/hal_nxp-3.6.0/mcux/mcux-sdk/CMSIS/DSP/Source/ComplexMathFunctions/ |
D | arm_cmplx_conj_q15.c | 61 q31_t in1; in arm_cmplx_conj_q15() local 93 in1 = *pSrc++; in arm_cmplx_conj_q15() 94 *pDst++ = __SSAT(-in1, 16); in arm_cmplx_conj_q15() 107 q31_t in1; /* Temporary input variable */ in arm_cmplx_conj_q15() local 126 in1 = read_q15x2_ia ((q15_t **) &pSrc); in arm_cmplx_conj_q15() 132 in1 = __QASX(0, in1); in arm_cmplx_conj_q15() 137 in1 = __QSAX(0, in1); in arm_cmplx_conj_q15() 143 in1 = ((uint32_t) in1 >> 16) | ((uint32_t) in1 << 16); in arm_cmplx_conj_q15() 148 write_q15x2_ia (&pDst, in1); in arm_cmplx_conj_q15() 154 in1 = *pSrc++; in arm_cmplx_conj_q15() [all …]
|
/hal_nxp-3.6.0/mcux/mcux-sdk/CMSIS/DSP/Source/FilteringFunctions/ |
D | arm_conv_partial_q7.c | 83 q15_t in1, in2; /* Temporary input variables */ in arm_conv_partial_q7() local 184 in1 = (q15_t) *px++; in arm_conv_partial_q7() 186 input1 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16); in arm_conv_partial_q7() 189 in1 = (q15_t) *py--; in arm_conv_partial_q7() 191 input2 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16); in arm_conv_partial_q7() 198 in1 = (q15_t) *px++; in arm_conv_partial_q7() 200 input1 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16); in arm_conv_partial_q7() 203 in1 = (q15_t) *py--; in arm_conv_partial_q7() 205 input2 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16); in arm_conv_partial_q7() 319 in1 = (q15_t) x0; in arm_conv_partial_q7() [all …]
|
D | arm_conv_q7.c | 242 q15_t in1, in2; /* Temporary input variables */ in arm_conv_q7() local 325 in1 = (q15_t) *px++; in arm_conv_q7() 327 input1 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16U); in arm_conv_q7() 330 in1 = (q15_t) *py--; in arm_conv_q7() 332 input2 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16U); in arm_conv_q7() 339 in1 = (q15_t) *px++; in arm_conv_q7() 341 input1 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16U); in arm_conv_q7() 344 in1 = (q15_t) *py--; in arm_conv_q7() 346 input2 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16U); in arm_conv_q7() 452 in1 = (q15_t) x0; in arm_conv_q7() [all …]
|
D | arm_correlate_q7.c | 287 q15_t in1, in2; /* Temporary input variables */ in arm_correlate_q7() local 398 in1 = (q15_t) *px++; in arm_correlate_q7() 400 input1 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16); in arm_correlate_q7() 403 in1 = (q15_t) *py++; in arm_correlate_q7() 405 input2 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16); in arm_correlate_q7() 412 in1 = (q15_t) *px++; in arm_correlate_q7() 414 input1 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16); in arm_correlate_q7() 417 in1 = (q15_t) *py++; in arm_correlate_q7() 419 input2 = ((q31_t) in1 & 0x0000FFFF) | ((q31_t) in2 << 16); in arm_correlate_q7() 527 in1 = (q15_t) x0; in arm_correlate_q7() [all …]
|
D | arm_fir_sparse_q15.c | 82 q31_t in1, in2; /* Temporary variables */ in arm_fir_sparse_q15() local 297 in1 = *pScr2++; in arm_fir_sparse_q15() 301 … write_q15x2_ia (&pOut, __PKHBT((q15_t) __SSAT(in1 >> 15, 16), (q15_t) __SSAT(in2 >> 15, 16), 16)); in arm_fir_sparse_q15() 303 … write_q15x2_ia (&pOut, __PKHBT((q15_t) __SSAT(in2 >> 15, 16), (q15_t) __SSAT(in1 >> 15, 16), 16)); in arm_fir_sparse_q15() 306 in1 = *pScr2++; in arm_fir_sparse_q15() 310 … write_q15x2_ia (&pOut, __PKHBT((q15_t) __SSAT(in1 >> 15, 16), (q15_t) __SSAT(in2 >> 15, 16), 16)); in arm_fir_sparse_q15() 312 … write_q15x2_ia (&pOut, __PKHBT((q15_t) __SSAT(in2 >> 15, 16), (q15_t) __SSAT(in1 >> 15, 16), 16)); in arm_fir_sparse_q15()
|
/hal_nxp-3.6.0/mcux/mcux-sdk/CMSIS/DSP/Source/BasicMathFunctions/ |
D | arm_shift_q15.c | 114 q15_t in1, in2; /* Temporary input variables */ in arm_shift_q15() local 129 in1 = *pSrc++; in arm_shift_q15() 134 write_q15x2_ia (&pDst, __PKHBT(__SSAT(((q31_t) in1 << shiftBits), 16), in arm_shift_q15() 138 __SSAT(((q31_t) in1 << shiftBits), 16), 16)); in arm_shift_q15() 142 in1 = *pSrc++; in arm_shift_q15() 146 write_q15x2_ia (&pDst, __PKHBT(__SSAT(((q31_t) in1 << shiftBits), 16), in arm_shift_q15() 150 __SSAT(((q31_t) in1 << shiftBits), 16), 16)); in arm_shift_q15() 172 in1 = *pSrc++; in arm_shift_q15() 177 write_q15x2_ia (&pDst, __PKHBT((in1 >> -shiftBits), in arm_shift_q15() 181 (in1 >> -shiftBits), 16)); in arm_shift_q15() [all …]
|
D | arm_negate_q15.c | 109 q31_t in1; /* Temporary input variables */ in arm_negate_q15() local 121 in1 = read_q15x2_ia ((q15_t **) &pSrc); in arm_negate_q15() 122 write_q15x2_ia (&pDst, __QSUB16(0, in1)); in arm_negate_q15() 124 in1 = read_q15x2_ia ((q15_t **) &pSrc); in arm_negate_q15() 125 write_q15x2_ia (&pDst, __QSUB16(0, in1)); in arm_negate_q15()
|
D | arm_shift_q7.c | 116 q7_t in1, in2, in3, in4; /* Temporary input variables */ in arm_shift_q7() local 131 in1 = *pSrc++; in arm_shift_q7() 137 write_q7x4_ia (&pDst, __PACKq7(__SSAT(((q15_t) in1 << shiftBits), 8), in arm_shift_q7() 160 in1 = *pSrc++; in arm_shift_q7() 166 write_q7x4_ia (&pDst, __PACKq7((in1 >> -shiftBits), in arm_shift_q7()
|
D | arm_negate_q7.c | 107 q31_t in1; /* Temporary input variable */ in arm_negate_q7() local 119 in1 = read_q7x4_ia ((q7_t **) &pSrc); in arm_negate_q7() 120 write_q7x4_ia (&pDst, __QSUB8(0, in1)); in arm_negate_q7()
|
D | arm_scale_f32.c | 167 float32_t in1, in2, in3, in4; in arm_scale_f32() local 172 in1 = (*pSrc++) * scale; in arm_scale_f32() 180 *pDst++ = in1; in arm_scale_f32()
|
D | arm_scale_q7.c | 123 q7_t in1, in2, in3, in4; /* Temporary input variables */ in arm_scale_q7() local 136 in1 = *pSrc++; in arm_scale_q7() 142 out1 = (q7_t) (__SSAT(((in1) * scaleFract) >> kShift, 8)); in arm_scale_q7()
|
D | arm_scale_q15.c | 124 q15_t in1, in2, in3, in4; /* Temporary input variables */ in arm_scale_q15() local 156 in1 = (q15_t) (__SSAT(out1, 16)); in arm_scale_q15() 162 write_q15x2_ia (&pDst, __PKHBT(in2, in1, 16)); in arm_scale_q15()
|
/hal_nxp-3.6.0/mcux/mcux-sdk/CMSIS/DSP/Source/SupportFunctions/ |
D | arm_q7_to_q15.c | 108 q31_t in1, in2; in arm_q7_to_q15() local 127 in1 = __SXTB16(__ROR(in, 8)); in arm_q7_to_q15() 132 in1 = in1 << 8U; in arm_q7_to_q15() 135 in1 = in1 & 0xFF00FF00; in arm_q7_to_q15() 139 out2 = __PKHTB(in1, in2, 16); in arm_q7_to_q15() 140 out1 = __PKHBT(in2, in1, 16); in arm_q7_to_q15() 142 out1 = __PKHTB(in1, in2, 16); in arm_q7_to_q15() 143 out2 = __PKHBT(in2, in1, 16); in arm_q7_to_q15()
|
D | arm_q15_to_q31.c | 106 q31_t in1, in2; in arm_q15_to_q31() local 120 in1 = read_q15x2_ia ((q15_t **) &pIn); in arm_q15_to_q31() 126 out1 = in1 << 16U; in arm_q15_to_q31() 128 out2 = in1 & 0xFFFF0000; in arm_q15_to_q31() 137 out1 = in1 & 0xFFFF0000; in arm_q15_to_q31() 139 out2 = in1 << 16U; in arm_q15_to_q31()
|
D | arm_q15_to_q7.c | 106 q31_t in1, in2; in arm_q15_to_q7() local 122 in1 = read_q15x2_ia ((q15_t **) &pIn); in arm_q15_to_q7() 127 out1 = __PKHTB(in2, in1, 16); in arm_q15_to_q7() 128 out2 = __PKHBT(in2, in1, 16); in arm_q15_to_q7() 132 out1 = __PKHTB(in1, in2, 16); in arm_q15_to_q7() 133 out2 = __PKHBT(in1, in2, 16); in arm_q15_to_q7()
|
D | arm_q31_to_q15.c | 109 q31_t in1, in2, in3, in4; in arm_q31_to_q15() local 125 in1 = *pIn++; in arm_q31_to_q15() 132 out1 = __PKHTB(in2, in1, 16); in arm_q31_to_q15() 135 out1 = __PKHTB(in1, in2, 16); in arm_q31_to_q15()
|
/hal_nxp-3.6.0/mcux/mcux-sdk/CMSIS/NN/Source/NNSupportFunctions/ |
D | arm_q7_to_q15_no_shift.c | 65 q31_t in1, in2; in arm_q7_to_q15_no_shift() local 77 in1 = __SXTB16(__ROR((uint32_t)in, 8)); in arm_q7_to_q15_no_shift() 83 out2 = (int32_t)__PKHTB(in1, in2, 16); in arm_q7_to_q15_no_shift() 84 out1 = (int32_t)__PKHBT(in2, in1, 16); in arm_q7_to_q15_no_shift() 86 out1 = (int32_t)__PKHTB(in1, in2, 16); in arm_q7_to_q15_no_shift() 87 out2 = (int32_t)__PKHBT(in2, in1, 16); in arm_q7_to_q15_no_shift()
|
D | arm_q7_to_q15_reordered_no_shift.c | 84 q31_t in1, in2; in arm_q7_to_q15_reordered_no_shift() local 100 in1 = __SXTB16(__ROR((uint32_t)in, 8)); in arm_q7_to_q15_reordered_no_shift() 107 *__SIMD32(pDst)++ = in1; in arm_q7_to_q15_reordered_no_shift() 109 *__SIMD32(pDst)++ = in1; in arm_q7_to_q15_reordered_no_shift()
|
/hal_nxp-3.6.0/mcux/mcux-sdk/CMSIS/DSP/Source/MatrixFunctions/ |
D | arm_mat_inverse_f32.c | 584 float32_t Xchg, in = 0.0f, in1; /* Temporary input values */ in arm_mat_inverse_f32() local 794 in1 = *pInT1; in arm_mat_inverse_f32() 795 *pInT1++ = in1 / in; in arm_mat_inverse_f32() 825 in1 = *pInT2; in arm_mat_inverse_f32() 826 *pInT2++ = in1 / in; in arm_mat_inverse_f32() 893 in1 = *pInT1; in arm_mat_inverse_f32() 894 *pInT1++ = in1 - (in * *pPRT_in++); in arm_mat_inverse_f32() 926 in1 = *pInT2; in arm_mat_inverse_f32() 927 *pInT2++ = in1 - (in * *pPRT_pDst++); in arm_mat_inverse_f32() 989 float32_t Xchg, in = 0.0f, in1; /* Temporary input values */ local [all …]
|
D | arm_mat_inverse_f64.c | 65 float64_t Xchg, in = 0.0, in1; /* Temporary input values */ local 260 in1 = *pInT1; 261 *pInT1++ = in1 / in; 274 in1 = *pInT2; 275 *pInT2++ = in1 / in; 323 in1 = *pInT1; 324 *pInT1++ = in1 - (in * *pPRT_in++); 338 in1 = *pInT2; 339 *pInT2++ = in1 - (in * *pPRT_pDst++);
|
D | arm_mat_inverse_f16.c | 565 _Float16 Xchg, in = 0.0f16, in1; /* Temporary input values */ in arm_mat_inverse_f16() local 757 in1 = *pInT1; in arm_mat_inverse_f16() 758 *pInT1++ = in1 / in; in arm_mat_inverse_f16() 771 in1 = *pInT2; in arm_mat_inverse_f16() 772 *pInT2++ = in1 / in; in arm_mat_inverse_f16() 820 in1 = *pInT1; in arm_mat_inverse_f16() 821 *pInT1++ = in1 - (in * *pPRT_in++); in arm_mat_inverse_f16() 835 in1 = *pInT2; in arm_mat_inverse_f16() 836 *pInT2++ = in1 - (in * *pPRT_pDst++); in arm_mat_inverse_f16()
|
D | arm_mat_scale_q15.c | 149 q15_t in1, in2, in3, in4; /* Temporary input variables */ in arm_mat_scale_q15() local 197 in1 = (q15_t) (__SSAT(out1, 16)); in arm_mat_scale_q15() 203 write_q15x2_ia (&pOut, __PKHBT(in2, in1, 16)); in arm_mat_scale_q15()
|
/hal_nxp-3.6.0/mcux/mcux-sdk/CMSIS/DSP/Source/StatisticsFunctions/ |
D | arm_power_q7.c | 111 … q31_t in1, in2; /* Temporary variables to store input value */ in arm_power_q7() local 127 in1 = __SXTB16(__ROR(in32, 8)); in arm_power_q7() 131 sum = __SMLAD(in1, in1, sum); in arm_power_q7()
|
/hal_nxp-3.6.0/mcux/mcux-sdk/CMSIS/DSP/Source/TransformFunctions/ |
D | arm_rfft_q31.c | 177 q31x4_t in1 = vld1q_s32(pIn1); in arm_split_rfft_q31() local 182 …q31x4_t out = vhaddq_s32(MVE_CMPLX_MULT_FX_AxB_S32(in1, coefA),MVE_CMPLX_MULT_FX_AxConjB_S… in arm_split_rfft_q31() 184 …q31x4_t out = vhaddq_s32(MVE_CMPLX_MULT_FX_AxB(in1, coefA),MVE_CMPLX_MULT_FX_AxConjB(coefB… in arm_split_rfft_q31() 333 q31x4_t in1 = vld1q_s32(pIn1); in arm_split_rifft_q31() local 340 q31x4_t out = vhaddq_s32(MVE_CMPLX_MULT_FX_AxConjB_S32(in1, coefA), in arm_split_rifft_q31() 343 q31x4_t out = vhaddq_s32(MVE_CMPLX_MULT_FX_AxConjB(in1, coefA), in arm_split_rifft_q31()
|
D | arm_rfft_q15.c | 182 q15x8_t in1 = vld1q_s16(pIn1); in arm_split_rfft_q15() local 188 q15x8_t out = vhaddq_s16(MVE_CMPLX_MULT_FX_AxB_S16(in1, coefA), in arm_split_rfft_q15() 191 q15x8_t out = vhaddq_s16(MVE_CMPLX_MULT_FX_AxB(in1, coefA), in arm_split_rfft_q15() 410 q15x8_t in1 = vld1q_s16(pIn1); in arm_split_rifft_q15() local 416 q15x8_t out = vhaddq_s16(MVE_CMPLX_MULT_FX_AxConjB(in1, coefA), in arm_split_rifft_q15()
|