Home
last modified time | relevance | path

Searched refs:res (Results 1 – 25 of 50) sorted by relevance

12

/hal_nxp-3.5.0/mcux/mcux-sdk/CMSIS/Include/
Dcmsis_iccarm.h555 uint32_t res; in __get_APSR() local
556 __asm("MRS %0,APSR" : "=r" (res)); in __get_APSR()
557 return res; in __get_APSR()
625 uint32_t res; in __get_MSPLIM() local
629 res = 0U; in __get_MSPLIM()
631 __asm volatile("MRS %0,MSPLIM" : "=r" (res)); in __get_MSPLIM()
633 return res; in __get_MSPLIM()
649 uint32_t res; in __get_PSPLIM() local
653 res = 0U; in __get_PSPLIM()
655 __asm volatile("MRS %0,PSPLIM" : "=r" (res)); in __get_PSPLIM()
[all …]
/hal_nxp-3.5.0/mcux/mcux-sdk/CMSIS/Core/Include/
Dcmsis_iccarm.h588 uint32_t res; in __get_APSR() local
589 __asm("MRS %0,APSR" : "=r" (res)); in __get_APSR()
590 return res; in __get_APSR()
658 uint32_t res; in __get_MSPLIM() local
662 res = 0U; in __get_MSPLIM()
664 __asm volatile("MRS %0,MSPLIM" : "=r" (res)); in __get_MSPLIM()
666 return res; in __get_MSPLIM()
682 uint32_t res; in __get_PSPLIM() local
686 res = 0U; in __get_PSPLIM()
688 __asm volatile("MRS %0,PSPLIM" : "=r" (res)); in __get_PSPLIM()
[all …]
/hal_nxp-3.5.0/mcux/mcux-sdk/CMSIS/DSP/Source/TransformFunctions/
Darm_rfft_fast_f16.c52 float16x8x2_t tmp1, tmp2, res; in stage_rfft_f16() local
130 res.val[0] = vmulq(tw.val[0], tmp2.val[0]); in stage_rfft_f16()
131 res.val[0] = vfmsq(res.val[0],tw.val[1], tmp2.val[1]); in stage_rfft_f16()
133 res.val[1] = vmulq(tw.val[0], tmp2.val[1]); in stage_rfft_f16()
134 res.val[1] = vfmaq(res.val[1], tw.val[1], tmp2.val[0]); in stage_rfft_f16()
136 res.val[0] = vaddq_f16(res.val[0],tmp1.val[0] ); in stage_rfft_f16()
137 res.val[1] = vaddq_f16(res.val[1],tmp1.val[1] ); in stage_rfft_f16()
139 res.val[0] = vmulq_n_f16(res.val[0], 0.5f); in stage_rfft_f16()
140 res.val[1] = vmulq_n_f16(res.val[1], 0.5f); in stage_rfft_f16()
143 vst2q_f16(pOut, res); in stage_rfft_f16()
[all …]
Darm_rfft_fast_f32.c47 float32x4x2_t tmp1, tmp2, res; in stage_rfft_f32() local
125 res.val[0] = vmulq(tw.val[0], tmp2.val[0]); in stage_rfft_f32()
126 res.val[0] = vfmsq(res.val[0],tw.val[1], tmp2.val[1]); in stage_rfft_f32()
128 res.val[1] = vmulq(tw.val[0], tmp2.val[1]); in stage_rfft_f32()
129 res.val[1] = vfmaq(res.val[1], tw.val[1], tmp2.val[0]); in stage_rfft_f32()
131 res.val[0] = vaddq_f32(res.val[0],tmp1.val[0] ); in stage_rfft_f32()
132 res.val[1] = vaddq_f32(res.val[1],tmp1.val[1] ); in stage_rfft_f32()
134 res.val[0] = vmulq_n_f32(res.val[0], 0.5f); in stage_rfft_f32()
135 res.val[1] = vmulq_n_f32(res.val[1], 0.5f); in stage_rfft_f32()
138 vst2q_f32(pOut, res); in stage_rfft_f32()
[all …]
/hal_nxp-3.5.0/mcux/mcux-sdk/CMSIS/DSP/Source/FilteringFunctions/
Darm_conv_f32.c341 float32x4_t res = vdupq_n_f32(0) ; in arm_conv_f32() local
356 res = vdupq_n_f32(0) ; in arm_conv_f32()
372 res = vmlaq_f32(res,vec1, vec2); in arm_conv_f32()
382 accum = vpadd_f32(vget_low_f32(res), vget_high_f32(res)); in arm_conv_f32()
476 float32x4_t res = vdupq_n_f32(0) ; in arm_conv_f32() local
496 res = vdupq_n_f32(0) ; in arm_conv_f32()
507 res = vmlaq_n_f32(res,x,c[3]); in arm_conv_f32()
511 res = vmlaq_n_f32(res,x,c[2]); in arm_conv_f32()
515 res = vmlaq_n_f32(res,x,c[1]); in arm_conv_f32()
519 res = vmlaq_n_f32(res,x,c[0]); in arm_conv_f32()
[all …]
Darm_correlate_f32.c436 float32x4_t res = vdupq_n_f32(0) ; in arm_correlate_f32() local
444 res = vmlaq_f32(res,x, y); in arm_correlate_f32()
453 accum = vpadd_f32(vget_low_f32(res), vget_high_f32(res)); in arm_correlate_f32()
553 float32x4_t res = vdupq_n_f32(0) ; in arm_correlate_f32() local
568 res = vdupq_n_f32(0) ; in arm_correlate_f32()
580 res = vmlaq_n_f32(res,x,c[0]); in arm_correlate_f32()
584 res = vmlaq_n_f32(res,x,c[1]); in arm_correlate_f32()
588 res = vmlaq_n_f32(res,x,c[2]); in arm_correlate_f32()
592 res = vmlaq_n_f32(res,x,c[3]); in arm_correlate_f32()
607 res = vmlaq_n_f32(res,x1v,c0); in arm_correlate_f32()
[all …]
/hal_nxp-3.5.0/mcux/mcux-sdk/CMSIS/NN/Source/ConvolutionFunctions/
Darm_convolve_1x1_s8_fast.c100 int32x4_t res = vldrwq_s32(temp_out); in arm_convolve_1x1_s8_fast() local
103 res = vaddq_n_s32(res, bias_data[i_out_ch]); in arm_convolve_1x1_s8_fast()
106 res = vaddq_n_s32(res, sum_row); in arm_convolve_1x1_s8_fast()
107 res = arm_requantize_mve(res, output_mult[i_out_ch], output_shift[i_out_ch]); in arm_convolve_1x1_s8_fast()
108 res = vaddq_n_s32(res, out_offset); in arm_convolve_1x1_s8_fast()
110 res = vmaxq_s32(res, vdupq_n_s32(out_activation_min)); in arm_convolve_1x1_s8_fast()
111 res = vminq_s32(res, vdupq_n_s32(out_activation_max)); in arm_convolve_1x1_s8_fast()
115 vstrbq_scatter_offset_s32(output_data, scatter_offset, res); in arm_convolve_1x1_s8_fast()
Darm_convolve_1_x_n_s8.c151 int32x4_t res = vldrwq_s32(acc); in arm_convolve_1_x_n_s8() local
153 res = vaddq_s32(res, s_offset); in arm_convolve_1_x_n_s8()
156 res = vaddq_n_s32(res, bias_data[i_out_ch]); in arm_convolve_1_x_n_s8()
158 res = arm_requantize_mve(res, output_mult[i_out_ch], output_shift[i_out_ch]); in arm_convolve_1_x_n_s8()
159 res = vaddq_n_s32(res, out_offset); in arm_convolve_1_x_n_s8()
161 res = vmaxq_s32(res, vdupq_n_s32(out_activation_min)); in arm_convolve_1_x_n_s8()
162 res = vminq_s32(res, vdupq_n_s32(out_activation_max)); in arm_convolve_1_x_n_s8()
165 vstrbq_scatter_offset_s32(output_data, scatter_offset, res); in arm_convolve_1_x_n_s8()
Darm_nn_mat_mult_s8.c104 int32x4_t res = {acc_0, acc_1, acc_2, acc_3}; in arm_nn_mat_mult_s8() local
107 res = vaddq_n_s32(res, bias[i_out_ch]); in arm_nn_mat_mult_s8()
109 res = arm_requantize_mve(res, output_mult[i_out_ch], output_shift[i_out_ch]); in arm_nn_mat_mult_s8()
110 res = vaddq_n_s32(res, out_offset); in arm_nn_mat_mult_s8()
112 res = vmaxq_s32(res, vdupq_n_s32(activation_min)); in arm_nn_mat_mult_s8()
113 res = vminq_s32(res, vdupq_n_s32(activation_max)); in arm_nn_mat_mult_s8()
116 vstrbq_scatter_offset_s32(&out[i_out_ch], scatter_offset, res); in arm_nn_mat_mult_s8()
Darm_convolve_s8.c138 int32x4_t res = vldrwq_s32(acc); in arm_convolve_s8() local
142 res = vaddq_n_s32(res, bias_data[i_out_ch]); in arm_convolve_s8()
144 res = vaddq_s32(res, s_offset); in arm_convolve_s8()
145 … res = arm_requantize_mve(res, output_mult[i_out_ch], output_shift[i_out_ch]); in arm_convolve_s8()
146 res = vaddq_n_s32(res, out_offset); in arm_convolve_s8()
148 res = vmaxq_s32(res, vdupq_n_s32(out_activation_min)); in arm_convolve_s8()
149 res = vminq_s32(res, vdupq_n_s32(out_activation_max)); in arm_convolve_s8()
152 vstrbq_scatter_offset_s32(out, scatter_offset, res); in arm_convolve_s8()
Darm_depthwise_conv_s8.c100 int32x4_t res = vldrwq_s32(out_buff); in depthwise_conv_s8_mult_4() local
101 res = arm_requantize_mve_32x4(res, in depthwise_conv_s8_mult_4()
104 res = vaddq_n_s32(res, output_offset); in depthwise_conv_s8_mult_4()
106 res = vmaxq_s32(res, vdupq_n_s32(output_activation_min)); in depthwise_conv_s8_mult_4()
107 res = vminq_s32(res, vdupq_n_s32(output_activation_max)); in depthwise_conv_s8_mult_4()
108 vstrbq_s32(output, res); in depthwise_conv_s8_mult_4()
/hal_nxp-3.5.0/mcux/mcux-sdk/CMSIS/RTOS2/RTX/Source/
Drtx_core_ca.h444 register uint32_t res; in atomic_wr8() local
460 [res] "=&l" (res) in atomic_wr8()
490 register uint32_t val, res; in atomic_set32() local
508 [res] "=&l" (res) in atomic_set32()
539 register uint32_t val, res; in atomic_clr32() local
557 [res] "=&l" (res) in atomic_clr32()
595 register uint32_t val, res; in atomic_chk32_all() local
621 [res] "=&l" (res) in atomic_chk32_all()
658 register uint32_t val, res; in atomic_chk32_any() local
683 [res] "=&l" (res) in atomic_chk32_any()
[all …]
Drtx_core_cm.h480 register uint32_t res; in atomic_wr8() local
497 [res] "=&l" (res) in atomic_wr8()
528 register uint32_t val, res; in atomic_set32() local
552 [res] "=&l" (res) in atomic_set32()
588 register uint32_t val, res; in atomic_clr32() local
612 [res] "=&l" (res) in atomic_clr32()
655 register uint32_t val, res; in atomic_chk32_all() local
691 [res] "=&l" (res) in atomic_chk32_all()
729 register uint32_t val, res; in atomic_chk32_any() local
759 [res] "=&l" (res) in atomic_chk32_any()
[all …]
/hal_nxp-3.5.0/mcux/mcux-sdk/CMSIS/NN/Source/SoftmaxFunctions/
Darm_softmax_s8.c128 int32x4_t res = MUL_SAT_MVE(ip, vdupq_n_s32(mult)); in arm_softmax_s8() local
130 res = arm_exp_on_negative_values_mve_32x4(res); in arm_softmax_s8()
131 res = DIV_POW2_MVE(res, ACCUM_BITS); in arm_softmax_s8()
132 res = vpselq_s32(res, vdupq_n_s32(0), p); in arm_softmax_s8()
133 sum += vaddvq_s32(res); in arm_softmax_s8()
194 const int32_t res = in arm_softmax_s8() local
196 output[tail_idx + i] = (int8_t)CLAMP(res, (int32_t)ACT_MAX, (int32_t)ACT_MIN); in arm_softmax_s8()
244 const int32_t res = in arm_softmax_s8()
246 output[col] = (int8_t)CLAMP(res, (int32_t)127, (int32_t)-128); in arm_softmax_s8()
/hal_nxp-3.5.0/mcux/mcux-sdk/CMSIS/DSP/Source/BasicMathFunctions/
Darm_abs_f16.c75 f16x8_t res; in arm_abs_f16() local
87 res = vabsq(vec1); in arm_abs_f16()
88 vst1q(pDst, res); in arm_abs_f16()
123 f16x8_t res; in arm_abs_f16() local
134 res = vabsq_f16(vec1); in arm_abs_f16()
135 vst1q_f16(pDst, res); in arm_abs_f16()
Darm_abs_f32.c75 f32x4_t res; in arm_abs_f32() local
87 res = vabsq(vec1); in arm_abs_f32()
88 vst1q(pDst, res); in arm_abs_f32()
122 f32x4_t res; in arm_abs_f32() local
133 res = vabsq_f32(vec1); in arm_abs_f32()
134 vst1q_f32(pDst, res); in arm_abs_f32()
Darm_negate_f32.c73 f32x4_t res; in arm_negate_f32() local
84 res = vnegq(vec1); in arm_negate_f32()
85 vst1q(pDst, res); in arm_negate_f32()
117 f32x4_t res; in arm_negate_f32() local
128 res = vnegq_f32(vec1); in arm_negate_f32()
129 vst1q_f32(pDst, res); in arm_negate_f32()
Darm_offset_f32.c76 f32x4_t res; in arm_offset_f32() local
86 res = vaddq(vec1,offset); in arm_offset_f32()
87 vst1q(pDst, res); in arm_offset_f32()
121 f32x4_t res; in arm_offset_f32() local
132 res = vaddq_f32(vec1,vdupq_n_f32(offset)); in arm_offset_f32()
133 vst1q_f32(pDst, res); in arm_offset_f32()
Darm_add_f32.c75 f32x4_t res; in arm_add_f32() local
87 res = vaddq(vec1, vec2); in arm_add_f32()
88 vst1q(pDst, res); in arm_add_f32()
125 f32x4_t res; in arm_add_f32() local
137 res = vaddq_f32(vec1, vec2); in arm_add_f32()
138 vst1q_f32(pDst, res); in arm_add_f32()
Darm_mult_f32.c75 f32x4_t res; in arm_mult_f32() local
86 res = vmulq(vec1, vec2); in arm_mult_f32()
87 vst1q(pDst, res); in arm_mult_f32()
123 f32x4_t res; in arm_mult_f32() local
135 res = vmulq_f32(vec1, vec2); in arm_mult_f32()
136 vst1q_f32(pDst, res); in arm_mult_f32()
Darm_sub_f32.c75 f32x4_t res; in arm_sub_f32() local
87 res = vsubq(vec1, vec2); in arm_sub_f32()
88 vst1q(pDst, res); in arm_sub_f32()
125 f32x4_t res; in arm_sub_f32() local
137 res = vsubq_f32(vec1, vec2); in arm_sub_f32()
138 vst1q_f32(pDst, res); in arm_sub_f32()
Darm_scale_f32.c89 f32x4_t res; in arm_scale_f32() local
100 res = vmulq(vec1,scale); in arm_scale_f32()
101 vst1q(pDst, res); in arm_scale_f32()
134 f32x4_t res; in arm_scale_f32() local
145 res = vmulq_f32(vec1, vdupq_n_f32(scale)); in arm_scale_f32()
146 vst1q_f32(pDst, res); in arm_scale_f32()
Darm_negate_f16.c73 f16x8_t res; in arm_negate_f16() local
84 res = vnegq(vec1); in arm_negate_f16()
85 vst1q(pDst, res); in arm_negate_f16()
Darm_scale_f16.c89 f16x8_t res; in arm_scale_f16() local
100 res = vmulq(vec1,scale); in arm_scale_f16()
101 vst1q(pDst, res); in arm_scale_f16()
Darm_offset_f16.c76 f16x8_t res; in arm_offset_f16() local
86 res = vaddq(vec1,offset); in arm_offset_f16()
87 vst1q(pDst, res); in arm_offset_f16()

12