/third_party/cmsis/CMSIS/DSP/Source/MatrixFunctions/ |
D | arm_mat_add_f32.c | 64 const arm_matrix_instance_f32 * pSrcA, in arm_mat_add_f32() argument 76 pDataA = pSrcA->pData; in arm_mat_add_f32() 84 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_add_f32() 85 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_add_f32() 86 (pSrcA->numRows != pDst->numRows) || (pSrcA->numCols != pDst->numCols)) in arm_mat_add_f32() 97 numSamples = (uint32_t) pSrcA->numRows * pSrcA->numCols; in arm_mat_add_f32() 142 const arm_matrix_instance_f32 * pSrcA, in arm_mat_add_f32() argument 146 float32_t *pIn1 = pSrcA->pData; /* input data matrix pointer A */ in arm_mat_add_f32() 157 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_add_f32() 158 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_add_f32() [all …]
|
D | arm_mat_sub_f32.c | 62 const arm_matrix_instance_f32 * pSrcA, in arm_mat_sub_f32() argument 74 pDataA = pSrcA->pData; in arm_mat_sub_f32() 82 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_sub_f32() 83 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_sub_f32() 84 (pSrcA->numRows != pDst->numRows) || (pSrcA->numCols != pDst->numCols)) in arm_mat_sub_f32() 95 numSamples = (uint32_t) pSrcA->numRows * pSrcA->numCols; in arm_mat_sub_f32() 136 const arm_matrix_instance_f32 * pSrcA, in arm_mat_sub_f32() argument 140 float32_t *pIn1 = pSrcA->pData; /* input data matrix pointer A */ in arm_mat_sub_f32() 151 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_sub_f32() 152 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_sub_f32() [all …]
|
D | arm_mat_sub_f16.c | 56 const arm_matrix_instance_f16 * pSrcA, in arm_mat_sub_f16() argument 68 pDataA = pSrcA->pData; in arm_mat_sub_f16() 76 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_sub_f16() 77 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_sub_f16() 78 (pSrcA->numRows != pDst->numRows) || (pSrcA->numCols != pDst->numCols)) in arm_mat_sub_f16() 89 numSamples = (uint32_t) pSrcA->numRows * pSrcA->numCols; in arm_mat_sub_f16() 130 const arm_matrix_instance_f16 * pSrcA, in arm_mat_sub_f16() argument 134 float16_t *pInA = pSrcA->pData; /* input data matrix pointer A */ in arm_mat_sub_f16() 145 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_sub_f16() 146 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_sub_f16() [all …]
|
D | arm_mat_add_f16.c | 58 const arm_matrix_instance_f16 * pSrcA, in arm_mat_add_f16() argument 70 pDataA = pSrcA->pData; in arm_mat_add_f16() 78 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_add_f16() 79 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_add_f16() 80 (pSrcA->numRows != pDst->numRows) || (pSrcA->numCols != pDst->numCols)) in arm_mat_add_f16() 91 numSamples = (uint32_t) pSrcA->numRows * pSrcA->numCols; in arm_mat_add_f16() 129 const arm_matrix_instance_f16 * pSrcA, in arm_mat_add_f16() argument 133 float16_t *pInA = pSrcA->pData; /* input data matrix pointer A */ in arm_mat_add_f16() 144 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_add_f16() 145 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_add_f16() [all …]
|
D | arm_mat_sub_q31.c | 55 const arm_matrix_instance_q31 * pSrcA, in arm_mat_sub_q31() argument 67 pDataA = pSrcA->pData; in arm_mat_sub_q31() 76 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_sub_q31() 77 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_sub_q31() 78 (pSrcA->numRows != pDst->numRows) || in arm_mat_sub_q31() 79 (pSrcA->numCols != pDst->numCols) ) in arm_mat_sub_q31() 92 numSamples = (uint32_t) pSrcA->numRows * pSrcA->numCols; in arm_mat_sub_q31() 133 const arm_matrix_instance_q31 * pSrcA, in arm_mat_sub_q31() argument 137 q31_t *pInA = pSrcA->pData; /* input data matrix pointer A */ in arm_mat_sub_q31() 148 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_sub_q31() [all …]
|
D | arm_mat_add_q31.c | 55 const arm_matrix_instance_q31 * pSrcA, in arm_mat_add_q31() argument 67 pDataA = pSrcA->pData; in arm_mat_add_q31() 76 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_add_q31() 77 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_add_q31() 78 (pSrcA->numRows != pDst->numRows) || in arm_mat_add_q31() 79 (pSrcA->numCols != pDst->numCols) ) in arm_mat_add_q31() 90 numSamples = (uint32_t) pSrcA->numRows * pSrcA->numCols; in arm_mat_add_q31() 131 const arm_matrix_instance_q31 * pSrcA, in arm_mat_add_q31() argument 135 q31_t *pInA = pSrcA->pData; /* input data matrix pointer A */ in arm_mat_add_q31() 146 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_add_q31() [all …]
|
D | arm_mat_sub_q15.c | 56 const arm_matrix_instance_q15 * pSrcA, in arm_mat_sub_q15() argument 69 pDataA = pSrcA->pData; in arm_mat_sub_q15() 78 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_sub_q15() 79 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_sub_q15() 80 (pSrcA->numRows != pDst->numRows) || in arm_mat_sub_q15() 81 (pSrcA->numCols != pDst->numCols) ) in arm_mat_sub_q15() 93 numSamples = (uint32_t) pSrcA->numRows * pSrcA->numCols; in arm_mat_sub_q15() 129 const arm_matrix_instance_q15 * pSrcA, in arm_mat_sub_q15() argument 133 q15_t *pInA = pSrcA->pData; /* input data matrix pointer A */ in arm_mat_sub_q15() 144 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_sub_q15() [all …]
|
D | arm_mat_add_q15.c | 56 const arm_matrix_instance_q15 * pSrcA, in arm_mat_add_q15() argument 68 pDataA = pSrcA->pData; in arm_mat_add_q15() 77 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_add_q15() 78 (pSrcA->numCols != pSrcB->numCols) || in arm_mat_add_q15() 79 (pSrcA->numRows != pDst->numRows) || in arm_mat_add_q15() 80 (pSrcA->numCols != pDst->numCols) ) in arm_mat_add_q15() 94 numSamples = (uint32_t) pSrcA->numRows * pSrcA->numCols; in arm_mat_add_q15() 132 const arm_matrix_instance_q15 * pSrcA, in arm_mat_add_q15() argument 136 q15_t *pInA = pSrcA->pData; /* input data matrix pointer A */ in arm_mat_add_q15() 147 if ((pSrcA->numRows != pSrcB->numRows) || in arm_mat_add_q15() [all …]
|
/third_party/cmsis/CMSIS/DSP/Source/ComplexMathFunctions/ |
D | arm_cmplx_mult_cmplx_f16.c | 76 const float16_t * pSrcA, in arm_cmplx_mult_cmplx_f16() argument 90 vecSrcA = vld1q(pSrcA); in arm_cmplx_mult_cmplx_f16() 92 pSrcA += 8; in arm_cmplx_mult_cmplx_f16() 97 vecSrcC = vld1q(pSrcA); in arm_cmplx_mult_cmplx_f16() 98 pSrcA += 8; in arm_cmplx_mult_cmplx_f16() 107 vecSrcA = vld1q(pSrcA); in arm_cmplx_mult_cmplx_f16() 108 pSrcA += 8; in arm_cmplx_mult_cmplx_f16() 123 vecSrcC = vld1q(pSrcA); in arm_cmplx_mult_cmplx_f16() 141 pSrcA += 8; in arm_cmplx_mult_cmplx_f16() 144 vecSrcA = vldrhq_z_f16(pSrcA, p); in arm_cmplx_mult_cmplx_f16() [all …]
|
D | arm_cmplx_dot_prod_q15.c | 59 const q15_t * pSrcA, in arm_cmplx_dot_prod_q15() argument 75 vecSrcA = vld1q(pSrcA); in arm_cmplx_dot_prod_q15() 77 pSrcA += 8; in arm_cmplx_dot_prod_q15() 83 vecSrcC = vld1q(pSrcA); in arm_cmplx_dot_prod_q15() 84 pSrcA += 8; in arm_cmplx_dot_prod_q15() 91 vecSrcA = vld1q(pSrcA); in arm_cmplx_dot_prod_q15() 92 pSrcA += 8; in arm_cmplx_dot_prod_q15() 105 vecSrcC = vld1q(pSrcA); in arm_cmplx_dot_prod_q15() 111 vecSrcA = vld1q(pSrcA); in arm_cmplx_dot_prod_q15() 123 pSrcA += 8; in arm_cmplx_dot_prod_q15() [all …]
|
D | arm_cmplx_dot_prod_q31.c | 61 const q31_t * pSrcA, in arm_cmplx_dot_prod_q31() argument 77 vecSrcA = vld1q(pSrcA); in arm_cmplx_dot_prod_q31() 79 pSrcA += 4; in arm_cmplx_dot_prod_q31() 85 vecSrcC = vld1q(pSrcA); in arm_cmplx_dot_prod_q31() 86 pSrcA += 4; in arm_cmplx_dot_prod_q31() 93 vecSrcA = vld1q(pSrcA); in arm_cmplx_dot_prod_q31() 94 pSrcA += 4; in arm_cmplx_dot_prod_q31() 107 vecSrcC = vld1q(pSrcA); in arm_cmplx_dot_prod_q31() 113 vecSrcA = vld1q(pSrcA); in arm_cmplx_dot_prod_q31() 125 pSrcA += 4; in arm_cmplx_dot_prod_q31() [all …]
|
D | arm_cmplx_mult_cmplx_f32.c | 74 const float32_t * pSrcA, in arm_cmplx_mult_cmplx_f32() argument 88 vecSrcA = vld1q(pSrcA); in arm_cmplx_mult_cmplx_f32() 90 pSrcA += 4; in arm_cmplx_mult_cmplx_f32() 95 vecSrcC = vld1q(pSrcA); in arm_cmplx_mult_cmplx_f32() 96 pSrcA += 4; in arm_cmplx_mult_cmplx_f32() 105 vecSrcA = vld1q(pSrcA); in arm_cmplx_mult_cmplx_f32() 106 pSrcA += 4; in arm_cmplx_mult_cmplx_f32() 121 vecSrcC = vld1q(pSrcA); in arm_cmplx_mult_cmplx_f32() 139 pSrcA += 4; in arm_cmplx_mult_cmplx_f32() 142 vecSrcA = vldrwq_z_f32(pSrcA, p); in arm_cmplx_mult_cmplx_f32() [all …]
|
D | arm_cmplx_dot_prod_f32.c | 80 const float32_t * pSrcA, in arm_cmplx_dot_prod_f32() argument 96 vecSrcA = vld1q(pSrcA); in arm_cmplx_dot_prod_f32() 98 pSrcA += 4; in arm_cmplx_dot_prod_f32() 103 vecSrcC = vld1q(pSrcA); in arm_cmplx_dot_prod_f32() 104 pSrcA += 4; in arm_cmplx_dot_prod_f32() 111 vecSrcA = vld1q(pSrcA); in arm_cmplx_dot_prod_f32() 112 pSrcA += 4; in arm_cmplx_dot_prod_f32() 125 vecSrcC = vld1q(pSrcA); in arm_cmplx_dot_prod_f32() 139 pSrcA += 4; in arm_cmplx_dot_prod_f32() 141 vecSrcA = vldrwq_z_f32(pSrcA, p); in arm_cmplx_dot_prod_f32() [all …]
|
D | arm_cmplx_dot_prod_f16.c | 85 const float16_t * pSrcA, in arm_cmplx_dot_prod_f16() argument 101 vecSrcA = vld1q( pSrcA); in arm_cmplx_dot_prod_f16() 103 pSrcA += 8; in arm_cmplx_dot_prod_f16() 108 vecSrcC = vld1q(pSrcA); in arm_cmplx_dot_prod_f16() 109 pSrcA += 8; in arm_cmplx_dot_prod_f16() 116 vecSrcA = vld1q(pSrcA); in arm_cmplx_dot_prod_f16() 117 pSrcA += 8; in arm_cmplx_dot_prod_f16() 130 vecSrcC = vld1q(pSrcA); in arm_cmplx_dot_prod_f16() 144 pSrcA += 8; in arm_cmplx_dot_prod_f16() 147 vecSrcA = vldrhq_z_f16(pSrcA, p); in arm_cmplx_dot_prod_f16() [all …]
|
D | arm_cmplx_mult_cmplx_q15.c | 55 const q15_t * pSrcA, in arm_cmplx_mult_cmplx_q15() argument 70 vecSrcA = vld1q(pSrcA); in arm_cmplx_mult_cmplx_q15() 72 pSrcA += 8; in arm_cmplx_mult_cmplx_q15() 80 vecSrcC = vld1q(pSrcA); in arm_cmplx_mult_cmplx_q15() 81 pSrcA += 8; in arm_cmplx_mult_cmplx_q15() 92 vecSrcA = vld1q(pSrcA); in arm_cmplx_mult_cmplx_q15() 93 pSrcA += 8; in arm_cmplx_mult_cmplx_q15() 110 vecSrcC = vld1q(pSrcA); in arm_cmplx_mult_cmplx_q15() 132 pSrcA += 8; in arm_cmplx_mult_cmplx_q15() 135 vecSrcA = vldrhq_z_s16(pSrcA, p); in arm_cmplx_mult_cmplx_q15() [all …]
|
D | arm_cmplx_mult_cmplx_q31.c | 55 const q31_t * pSrcA, in arm_cmplx_mult_cmplx_q31() argument 69 vecSrcA = vld1q(pSrcA); in arm_cmplx_mult_cmplx_q31() 71 pSrcA += 4; in arm_cmplx_mult_cmplx_q31() 78 vecSrcC = vld1q(pSrcA); in arm_cmplx_mult_cmplx_q31() 79 pSrcA += 4; in arm_cmplx_mult_cmplx_q31() 90 vecSrcA = vld1q(pSrcA); in arm_cmplx_mult_cmplx_q31() 91 pSrcA += 4; in arm_cmplx_mult_cmplx_q31() 108 vecSrcC = vld1q(pSrcA); in arm_cmplx_mult_cmplx_q31() 129 pSrcA += 4; in arm_cmplx_mult_cmplx_q31() 132 vecSrcA = vldrwq_z_s32(pSrcA, p); in arm_cmplx_mult_cmplx_q31() [all …]
|
/third_party/cmsis/CMSIS/DSP/Include/dsp/ |
D | basic_math_functions.h | 54 const q7_t * pSrcA, 68 const q15_t * pSrcA, 82 const q31_t * pSrcA, 96 const float32_t * pSrcA, 111 const float32_t * pSrcA, 126 const q7_t * pSrcA, 140 const q15_t * pSrcA, 154 const q31_t * pSrcA, 168 const float32_t * pSrcA, 183 const q7_t * pSrcA, [all …]
|
/third_party/cmsis/CMSIS/DSP/Source/BasicMathFunctions/ |
D | arm_mult_q7.c | 57 const q7_t * pSrcA, in arm_mult_q7() argument 73 vecA = vld1q(pSrcA); in arm_mult_q7() 83 pSrcA += 16; in arm_mult_q7() 94 vecA = vld1q(pSrcA); in arm_mult_q7() 102 const q7_t * pSrcA, in arm_mult_q7() argument 124 out1 = (q7_t) __SSAT((((q15_t) (*pSrcA++) * (*pSrcB++)) >> 7), 8); in arm_mult_q7() 125 out2 = (q7_t) __SSAT((((q15_t) (*pSrcA++) * (*pSrcB++)) >> 7), 8); in arm_mult_q7() 126 out3 = (q7_t) __SSAT((((q15_t) (*pSrcA++) * (*pSrcB++)) >> 7), 8); in arm_mult_q7() 127 out4 = (q7_t) __SSAT((((q15_t) (*pSrcA++) * (*pSrcB++)) >> 7), 8); in arm_mult_q7() 132 *pDst++ = (q7_t) __SSAT((((q15_t) (*pSrcA++) * (*pSrcB++)) >> 7), 8); in arm_mult_q7() [all …]
|
D | arm_sub_q15.c | 58 const q15_t * pSrcA, in arm_sub_q15() argument 75 vecA = vld1q(pSrcA); in arm_sub_q15() 85 pSrcA += 8; in arm_sub_q15() 96 vecA = vld1q(pSrcA); in arm_sub_q15() 105 const q15_t * pSrcA, in arm_sub_q15() argument 128 inA1 = read_q15x2_ia ((q15_t **) &pSrcA); in arm_sub_q15() 129 inA2 = read_q15x2_ia ((q15_t **) &pSrcA); in arm_sub_q15() 138 *pDst++ = (q15_t) __SSAT(((q31_t) *pSrcA++ - *pSrcB++), 16); in arm_sub_q15() 139 *pDst++ = (q15_t) __SSAT(((q31_t) *pSrcA++ - *pSrcB++), 16); in arm_sub_q15() 140 *pDst++ = (q15_t) __SSAT(((q31_t) *pSrcA++ - *pSrcB++), 16); in arm_sub_q15() [all …]
|
D | arm_add_q15.c | 58 const q15_t * pSrcA, in arm_add_q15() argument 75 vecA = vld1q(pSrcA); in arm_add_q15() 85 pSrcA += 8; in arm_add_q15() 96 vecA = vld1q(pSrcA); in arm_add_q15() 104 const q15_t * pSrcA, in arm_add_q15() argument 127 inA1 = read_q15x2_ia ((q15_t **) &pSrcA); in arm_add_q15() 128 inA2 = read_q15x2_ia ((q15_t **) &pSrcA); in arm_add_q15() 137 *pDst++ = (q15_t) __SSAT(((q31_t) *pSrcA++ + *pSrcB++), 16); in arm_add_q15() 138 *pDst++ = (q15_t) __SSAT(((q31_t) *pSrcA++ + *pSrcB++), 16); in arm_add_q15() 139 *pDst++ = (q15_t) __SSAT(((q31_t) *pSrcA++ + *pSrcB++), 16); in arm_add_q15() [all …]
|
D | arm_dot_prod_f32.c | 68 const float32_t * pSrcA, in arm_dot_prod_f32() argument 88 vecA = vld1q(pSrcA); in arm_dot_prod_f32() 89 pSrcA += 4; in arm_dot_prod_f32() 108 vecA = vld1q(pSrcA); in arm_dot_prod_f32() 123 const float32_t * pSrcA, in arm_dot_prod_f32() argument 140 vec1 = vld1q_f32(pSrcA); in arm_dot_prod_f32() 151 pSrcA += 4; in arm_dot_prod_f32() 154 vec1 = vld1q_f32(pSrcA); in arm_dot_prod_f32() 185 sum += (*pSrcA++) * (*pSrcB++); in arm_dot_prod_f32() 187 sum += (*pSrcA++) * (*pSrcB++); in arm_dot_prod_f32() [all …]
|
D | arm_mult_f32.c | 66 const float32_t * pSrcA, in arm_mult_f32() argument 84 vec1 = vld1q(pSrcA); in arm_mult_f32() 90 pSrcA += 4; in arm_mult_f32() 104 vec1 = vld1q(pSrcA); in arm_mult_f32() 113 const float32_t * pSrcA, in arm_mult_f32() argument 133 vec1 = vld1q_f32(pSrcA); in arm_mult_f32() 139 pSrcA += 4; in arm_mult_f32() 161 *pDst++ = (*pSrcA++) * (*pSrcB++); in arm_mult_f32() 163 *pDst++ = (*pSrcA++) * (*pSrcB++); in arm_mult_f32() 165 *pDst++ = (*pSrcA++) * (*pSrcB++); in arm_mult_f32() [all …]
|
D | arm_add_f32.c | 66 const float32_t * pSrcA, in arm_add_f32() argument 85 vec1 = vld1q(pSrcA); in arm_add_f32() 91 pSrcA += 4; in arm_add_f32() 106 vec1 = vld1q(pSrcA); in arm_add_f32() 115 const float32_t * pSrcA, in arm_add_f32() argument 135 vec1 = vld1q_f32(pSrcA); in arm_add_f32() 141 pSrcA += 4; in arm_add_f32() 163 *pDst++ = (*pSrcA++) + (*pSrcB++); in arm_add_f32() 164 *pDst++ = (*pSrcA++) + (*pSrcB++); in arm_add_f32() 165 *pDst++ = (*pSrcA++) + (*pSrcB++); in arm_add_f32() [all …]
|
D | arm_dot_prod_q15.c | 60 const q15_t * pSrcA, in arm_dot_prod_q15() argument 78 vecA = vld1q(pSrcA); in arm_dot_prod_q15() 88 pSrcA += 8; in arm_dot_prod_q15() 98 vecA = vld1q(pSrcA); in arm_dot_prod_q15() 108 const q15_t * pSrcA, in arm_dot_prod_q15() argument 127 sum = __SMLALD(read_q15x2_ia ((q15_t **) &pSrcA), read_q15x2_ia ((q15_t **) &pSrcB), sum); in arm_dot_prod_q15() 128 sum = __SMLALD(read_q15x2_ia ((q15_t **) &pSrcA), read_q15x2_ia ((q15_t **) &pSrcB), sum); in arm_dot_prod_q15() 130 sum += (q63_t)((q31_t) *pSrcA++ * *pSrcB++); in arm_dot_prod_q15() 131 sum += (q63_t)((q31_t) *pSrcA++ * *pSrcB++); in arm_dot_prod_q15() 132 sum += (q63_t)((q31_t) *pSrcA++ * *pSrcB++); in arm_dot_prod_q15() [all …]
|
D | arm_sub_f32.c | 66 const float32_t * pSrcA, in arm_sub_f32() argument 85 vec1 = vld1q(pSrcA); in arm_sub_f32() 91 pSrcA += 4; in arm_sub_f32() 106 vec1 = vld1q(pSrcA); in arm_sub_f32() 115 const float32_t * pSrcA, in arm_sub_f32() argument 135 vec1 = vld1q_f32(pSrcA); in arm_sub_f32() 141 pSrcA += 4; in arm_sub_f32() 163 *pDst++ = (*pSrcA++) - (*pSrcB++); in arm_sub_f32() 165 *pDst++ = (*pSrcA++) - (*pSrcB++); in arm_sub_f32() 167 *pDst++ = (*pSrcA++) - (*pSrcB++); in arm_sub_f32() [all …]
|