/cmsis-dsp-latest/Source/FilteringFunctions/ |
D | arm_fir_fast_q15.c | 76 …q31_t x0, x1, x2, c0; /* Temporary variables to hold state and coefficien… in arm_fir_fast_q15() local 138 x1 = __PKHBT(x2, x0, 0); in arm_fir_fast_q15() 140 x1 = __PKHBT(x0, x2, 0); in arm_fir_fast_q15() 147 acc1 = __SMLADX(x1, c0, acc1); in arm_fir_fast_q15() 151 x1 = __PKHBT(x0, x2, 0); in arm_fir_fast_q15() 153 x1 = __PKHBT(x2, x0, 0); in arm_fir_fast_q15() 157 acc3 = __SMLADX(x1, c0, acc3); in arm_fir_fast_q15() 172 acc1 = __SMLADX(x1, c0, acc1); in arm_fir_fast_q15() 176 x1 = __PKHBT(x2, x0, 0); in arm_fir_fast_q15() 178 x1 = __PKHBT(x0, x2, 0); in arm_fir_fast_q15() [all …]
|
D | arm_fir_decimate_fast_q15.c | 72 …q31_t x0, x1, c0; /* Temporary variables to hold state and coefficien… in arm_fir_decimate_fast_q15() local 126 x1 = read_q15x2_ia (&px1); in arm_fir_decimate_fast_q15() 130 acc1 = __SMLAD(x1, c0, acc1); in arm_fir_decimate_fast_q15() 137 x1 = read_q15x2_ia (&px1); in arm_fir_decimate_fast_q15() 141 acc1 = __SMLAD(x1, c0, acc1); in arm_fir_decimate_fast_q15() 164 x1 = *px1++; in arm_fir_decimate_fast_q15() 168 acc1 = __SMLAD(x1, c0, acc1); in arm_fir_decimate_fast_q15() 318 …q15_t x0, x1, c0; /* Temporary variables to hold state and coefficien… in arm_fir_decimate_fast_q15() local 369 x1 = *px1++; in arm_fir_decimate_fast_q15() 373 acc1 += x1 * c0; in arm_fir_decimate_fast_q15() [all …]
|
D | arm_conv_partial_opt_q15.c | 75 …q31_t x1; /* Temporary variables to hold state and coefficien… in arm_conv_partial_opt_q15() local 220 x1 = read_q15x2_ia (&pScr1); in arm_conv_partial_opt_q15() 235 acc0 = __SMLALD(x1, y1, acc0); in arm_conv_partial_opt_q15() 240 x3 = __PKHBT(x2, x1, 0); in arm_conv_partial_opt_q15() 242 x3 = __PKHBT(x1, x2, 0); in arm_conv_partial_opt_q15() 249 x1 = read_q15x2_ia (&pScr1); in arm_conv_partial_opt_q15() 253 acc2 = __SMLALD(x1, y2, acc2); in arm_conv_partial_opt_q15() 257 x3 = __PKHBT(x1, x2, 0); in arm_conv_partial_opt_q15() 259 x3 = __PKHBT(x2, x1, 0); in arm_conv_partial_opt_q15() 268 x3 = __PKHBT(x2, x1, 0); in arm_conv_partial_opt_q15() [all …]
|
D | arm_conv_partial_fast_opt_q15.c | 81 …q31_t x1; /* Temporary variables to hold state and coefficien… in arm_conv_partial_fast_opt_q15() local 219 x1 = read_q15x2_ia (&pScr1); in arm_conv_partial_fast_opt_q15() 234 acc0 = __SMLAD(x1, y1, acc0); in arm_conv_partial_fast_opt_q15() 239 x3 = __PKHBT(x2, x1, 0); in arm_conv_partial_fast_opt_q15() 241 x3 = __PKHBT(x1, x2, 0); in arm_conv_partial_fast_opt_q15() 248 x1 = read_q15x2_ia (&pScr1); in arm_conv_partial_fast_opt_q15() 252 acc2 = __SMLAD(x1, y2, acc2); in arm_conv_partial_fast_opt_q15() 256 x3 = __PKHBT(x1, x2, 0); in arm_conv_partial_fast_opt_q15() 258 x3 = __PKHBT(x2, x1, 0); in arm_conv_partial_fast_opt_q15() 267 x3 = __PKHBT(x2, x1, 0); in arm_conv_partial_fast_opt_q15() [all …]
|
D | arm_conv_partial_opt_q7.c | 74 q31_t x1, x2, x3, y1; /* Temporary input variables */ in arm_conv_partial_opt_q7() local 232 x1 = read_q15x2_ia (&pScr1); in arm_conv_partial_opt_q7() 245 acc0 = __SMLAD(x1, y1, acc0); in arm_conv_partial_opt_q7() 250 x3 = __PKHBT(x2, x1, 0); in arm_conv_partial_opt_q7() 252 x3 = __PKHBT(x1, x2, 0); in arm_conv_partial_opt_q7() 259 x1 = read_q15x2_ia (&pScr1); in arm_conv_partial_opt_q7() 263 x3 = __PKHBT(x1, x2, 0); in arm_conv_partial_opt_q7() 265 x3 = __PKHBT(x2, x1, 0); in arm_conv_partial_opt_q7() 275 acc2 = __SMLAD(x1, y1, acc2); in arm_conv_partial_opt_q7() 282 x3 = __PKHBT(x2, x1, 0); in arm_conv_partial_opt_q7() [all …]
|
D | arm_correlate_opt_q15.c | 80 …q31_t x1, x2, x3; /* Temporary variables for holding input1 and input… in arm_correlate_opt_q15() local 181 x1 = read_q15x2_ia (&pScr1); in arm_correlate_opt_q15() 195 acc0 = __SMLALD(x1, y1, acc0); in arm_correlate_opt_q15() 200 x3 = __PKHBT(x2, x1, 0); in arm_correlate_opt_q15() 202 x3 = __PKHBT(x1, x2, 0); in arm_correlate_opt_q15() 209 x1 = read_q15x2_ia (&pScr1); in arm_correlate_opt_q15() 213 acc2 = __SMLALD(x1, y2, acc2); in arm_correlate_opt_q15() 217 x3 = __PKHBT(x1, x2, 0); in arm_correlate_opt_q15() 219 x3 = __PKHBT(x2, x1, 0); in arm_correlate_opt_q15() 228 x3 = __PKHBT(x2, x1, 0); in arm_correlate_opt_q15() [all …]
|
D | arm_conv_fast_opt_q15.c | 86 …q31_t x1, x2, x3; /* Temporary variables to hold state and coefficien… in arm_conv_fast_opt_q15() local 208 x1 = read_q15x2_ia (&pScr1); in arm_conv_fast_opt_q15() 223 acc0 = __SMLAD(x1, y1, acc0); in arm_conv_fast_opt_q15() 228 x3 = __PKHBT(x2, x1, 0); in arm_conv_fast_opt_q15() 230 x3 = __PKHBT(x1, x2, 0); in arm_conv_fast_opt_q15() 237 x1 = read_q15x2_ia (&pScr1); in arm_conv_fast_opt_q15() 241 acc2 = __SMLAD(x1, y2, acc2); in arm_conv_fast_opt_q15() 245 x3 = __PKHBT(x1, x2, 0); in arm_conv_fast_opt_q15() 247 x3 = __PKHBT(x2, x1, 0); in arm_conv_fast_opt_q15() 256 x3 = __PKHBT(x2, x1, 0); in arm_conv_fast_opt_q15() [all …]
|
D | arm_conv_opt_q15.c | 82 …q31_t x1, x2, x3; /* Temporary variables to hold state and coefficien… in arm_conv_opt_q15() local 204 x1 = read_q15x2_ia (&pScr1); in arm_conv_opt_q15() 219 acc0 = __SMLALD(x1, y1, acc0); in arm_conv_opt_q15() 224 x3 = __PKHBT(x2, x1, 0); in arm_conv_opt_q15() 226 x3 = __PKHBT(x1, x2, 0); in arm_conv_opt_q15() 233 x1 = read_q15x2_ia (&pScr1); in arm_conv_opt_q15() 237 acc2 = __SMLALD(x1, y2, acc2); in arm_conv_opt_q15() 241 x3 = __PKHBT(x1, x2, 0); in arm_conv_opt_q15() 243 x3 = __PKHBT(x2, x1, 0); in arm_conv_opt_q15() 252 x3 = __PKHBT(x2, x1, 0); in arm_conv_opt_q15() [all …]
|
D | arm_correlate_fast_opt_q15.c | 83 …q31_t x1, x2, x3; /* Temporary variables for holding input and coeffi… in arm_correlate_fast_opt_q15() local 186 x1 = read_q15x2_ia (&pScr1); in arm_correlate_fast_opt_q15() 200 acc0 = __SMLAD(x1, y1, acc0); in arm_correlate_fast_opt_q15() 205 x3 = __PKHBT(x2, x1, 0); in arm_correlate_fast_opt_q15() 207 x3 = __PKHBT(x1, x2, 0); in arm_correlate_fast_opt_q15() 214 x1 = read_q15x2_ia (&pScr1); in arm_correlate_fast_opt_q15() 218 acc2 = __SMLAD(x1, y2, acc2); in arm_correlate_fast_opt_q15() 222 x3 = __PKHBT(x1, x2, 0); in arm_correlate_fast_opt_q15() 224 x3 = __PKHBT(x2, x1, 0); in arm_correlate_fast_opt_q15() 233 x3 = __PKHBT(x2, x1, 0); in arm_correlate_fast_opt_q15() [all …]
|
D | arm_fir_fast_q31.c | 77 …q31_t x0, x1, x2, x3, c0; /* Temporary variables to hold state and coefficien… in arm_fir_fast_q31() local 119 x1 = *px++; in arm_fir_fast_q31() 139 multAcc_32x32_keep32_R(acc1, x1, c0); in arm_fir_fast_q31() 154 multAcc_32x32_keep32_R(acc0, x1, c0); in arm_fir_fast_q31() 163 x1 = *(px + 2U); in arm_fir_fast_q31() 169 multAcc_32x32_keep32_R(acc3, x1, c0); in arm_fir_fast_q31() 180 multAcc_32x32_keep32_R(acc2, x1, c0); in arm_fir_fast_q31() 204 multAcc_32x32_keep32_R(acc1, x1, c0); in arm_fir_fast_q31() 209 x0 = x1; in arm_fir_fast_q31() 210 x1 = x2; in arm_fir_fast_q31()
|
D | arm_conv_opt_q7.c | 74 q31_t x1, x2, x3, y1; /* Temporary input variables */ in arm_conv_opt_q7() local 213 x1 = read_q15x2_ia (&pScr1); in arm_conv_opt_q7() 226 acc0 = __SMLAD(x1, y1, acc0); in arm_conv_opt_q7() 231 x3 = __PKHBT(x2, x1, 0); in arm_conv_opt_q7() 233 x3 = __PKHBT(x1, x2, 0); in arm_conv_opt_q7() 240 x1 = read_q15x2_ia (&pScr1); in arm_conv_opt_q7() 244 x3 = __PKHBT(x1, x2, 0); in arm_conv_opt_q7() 246 x3 = __PKHBT(x2, x1, 0); in arm_conv_opt_q7() 256 acc2 = __SMLAD(x1, y1, acc2); in arm_conv_opt_q7() 263 x3 = __PKHBT(x2, x1, 0); in arm_conv_opt_q7() [all …]
|
D | arm_fir_decimate_f64.c | 66 float64_t x1, x2, x3; in arm_fir_decimate_f64() local 117 x1 = *(px1++); in arm_fir_decimate_f64() 125 acc1 += x1 * c0; in arm_fir_decimate_f64() 134 x1 = *(px1++); in arm_fir_decimate_f64() 140 acc1 += x1 * c0; in arm_fir_decimate_f64() 149 x1 = *(px1++); in arm_fir_decimate_f64() 155 acc1 += x1 * c0; in arm_fir_decimate_f64() 164 x1 = *(px1++); in arm_fir_decimate_f64() 170 acc1 += x1 * c0; in arm_fir_decimate_f64() 188 x1 = *(px1++); in arm_fir_decimate_f64() [all …]
|
D | arm_correlate_opt_q7.c | 76 q31_t x1, x2, x3, y1; /* Temporary input variables */ in arm_correlate_opt_q7() local 238 x1 = read_q15x2_ia (&pScr1); in arm_correlate_opt_q7() 251 acc0 = __SMLAD(x1, y1, acc0); in arm_correlate_opt_q7() 256 x3 = __PKHBT(x2, x1, 0); in arm_correlate_opt_q7() 258 x3 = __PKHBT(x1, x2, 0); in arm_correlate_opt_q7() 265 x1 = read_q15x2_ia (&pScr1); in arm_correlate_opt_q7() 269 x3 = __PKHBT(x1, x2, 0); in arm_correlate_opt_q7() 271 x3 = __PKHBT(x2, x1, 0); in arm_correlate_opt_q7() 281 acc2 = __SMLAD(x1, y1, acc2); in arm_correlate_opt_q7() 288 x3 = __PKHBT(x2, x1, 0); in arm_correlate_opt_q7() [all …]
|
D | arm_fir_decimate_fast_q31.c | 79 q31_t x1, x2, x3; in arm_fir_decimate_fast_q31() local 130 x1 = *(px1++); in arm_fir_decimate_fast_q31() 138 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_fir_decimate_fast_q31() 147 x1 = *(px1++); in arm_fir_decimate_fast_q31() 153 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_fir_decimate_fast_q31() 162 x1 = *(px1++); in arm_fir_decimate_fast_q31() 168 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_fir_decimate_fast_q31() 177 x1 = *(px1++); in arm_fir_decimate_fast_q31() 183 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_fir_decimate_fast_q31() 201 x1 = *(px1++); in arm_fir_decimate_fast_q31() [all …]
|
D | arm_fir_decimate_q15.c | 329 …q31_t x0, x1, c0; /* Temporary variables to hold state and coefficien… in arm_fir_decimate_q15() local 383 x1 = read_q15x2_ia (&px1); in arm_fir_decimate_q15() 387 acc1 = __SMLALD(x1, c0, acc1); in arm_fir_decimate_q15() 394 x1 = read_q15x2_ia (&px1); in arm_fir_decimate_q15() 398 acc1 = __SMLALD(x1, c0, acc1); in arm_fir_decimate_q15() 421 x1 = *px1++; in arm_fir_decimate_q15() 425 acc1 = __SMLALD(x1, c0, acc1); in arm_fir_decimate_q15() 574 …q15_t x0, x1, c0; /* Temporary variables to hold state and coefficien… in arm_fir_decimate_q15() local 625 x1 = *px1++; in arm_fir_decimate_q15() 629 acc1 += x1 * c0; in arm_fir_decimate_q15() [all …]
|
D | arm_fir_f32.c | 706 float32x4_t accv0,accv1,samples0,samples1,x0,x1,x2,xa,xb,b; in arm_fir_f32() local 746 x1 = vld1q_f32(px + 4); in arm_fir_f32() 754 xb = x1; in arm_fir_f32() 758 xa = vextq_f32(x0,x1,1); in arm_fir_f32() 759 xb = vextq_f32(x1,x2,1); in arm_fir_f32() 764 xa = vextq_f32(x0,x1,2); in arm_fir_f32() 765 xb = vextq_f32(x1,x2,2); in arm_fir_f32() 770 xa = vextq_f32(x0,x1,3); in arm_fir_f32() 771 xb = vextq_f32(x1,x2,3); in arm_fir_f32() 777 x0 = x1; in arm_fir_f32() [all …]
|
D | arm_fir_q15.c | 475 …q31_t x0, x1, x2, c0; /* Temporary variables to hold state and coefficien… in arm_fir_q15() local 537 x1 = __PKHBT(x2, x0, 0); in arm_fir_q15() 539 x1 = __PKHBT(x0, x2, 0); in arm_fir_q15() 546 acc1 = __SMLALDX(x1, c0, acc1); in arm_fir_q15() 550 x1 = __PKHBT(x0, x2, 0); in arm_fir_q15() 552 x1 = __PKHBT(x2, x0, 0); in arm_fir_q15() 556 acc3 = __SMLALDX(x1, c0, acc3); in arm_fir_q15() 571 acc1 = __SMLALDX(x1, c0, acc1); in arm_fir_q15() 575 x1 = __PKHBT(x2, x0, 0); in arm_fir_q15() 577 x1 = __PKHBT(x0, x2, 0); in arm_fir_q15() [all …]
|
D | arm_conv_partial_f32.c | 109 float32_t x0, x1, x2, x3, c0; /* Temporary variables */ in arm_conv_partial_f32() local 309 x1 = *px++; in arm_conv_partial_f32() 328 acc1 += x1 * c0; in arm_conv_partial_f32() 341 acc0 += x1 * c0; in arm_conv_partial_f32() 352 x1 = *px++; in arm_conv_partial_f32() 362 acc3 += x1 * c0; in arm_conv_partial_f32() 375 acc2 += x1 * c0; in arm_conv_partial_f32() 396 acc1 += x1 * c0; in arm_conv_partial_f32() 403 x0 = x1; in arm_conv_partial_f32() 404 x1 = x2; in arm_conv_partial_f32()
|
D | arm_conv_fast_q31.c | 76 …q31_t x0, x1, x2, x3, c0; /* Temporary variables to hold state and coefficien… in arm_conv_fast_q31() local 248 x1 = *px++; in arm_conv_fast_q31() 267 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_fast_q31() 281 acc0 = (q31_t) ((((q63_t) acc0 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_fast_q31() 293 x1 = *px++; in arm_conv_fast_q31() 303 acc3 = (q31_t) ((((q63_t) acc3 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_fast_q31() 317 acc2 = (q31_t) ((((q63_t) acc2 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_fast_q31() 339 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_fast_q31() 346 x0 = x1; in arm_conv_fast_q31() 347 x1 = x2; in arm_conv_fast_q31()
|
D | arm_correlate_fast_q15.c | 76 …q31_t x0, x1, x2, x3, c0; /* Temporary variables for holding input and coeffi… in arm_correlate_fast_q15() local 272 x1 = read_q15x2 ((q15_t *) px + 1); in arm_correlate_fast_q15() 290 acc1 = __SMLAD(x1, c0, acc1); in arm_correlate_fast_q15() 317 x1 = read_q15x2 ((q15_t *) px + 3); in arm_correlate_fast_q15() 324 acc3 = __SMLAD(x1, c0, acc3); in arm_correlate_fast_q15() 352 acc1 = __SMLAD (x1, c0, acc1); in arm_correlate_fast_q15() 353 acc2 = __SMLADX(x1, c0, acc2); in arm_correlate_fast_q15() 371 acc1 = __SMLAD(x1, c0, acc1); in arm_correlate_fast_q15() 389 acc1 = __SMLAD(x1, c0, acc1); in arm_correlate_fast_q15() 406 acc0 = __SMLADX(x1, c0, acc0); in arm_correlate_fast_q15()
|
D | arm_correlate_fast_q31.c | 78 …q31_t x0, x1, x2, x3, c0; /* Temporary variables for holding input and coeffi… in arm_correlate_fast_q31() local 274 x1 = *px++; in arm_correlate_fast_q31() 293 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_correlate_fast_q31() 307 acc0 = (q31_t) ((((q63_t) acc0 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_correlate_fast_q31() 319 x1 = *px++; in arm_correlate_fast_q31() 329 acc3 = (q31_t) ((((q63_t) acc3 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_correlate_fast_q31() 343 acc2 = (q31_t) ((((q63_t) acc2 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_correlate_fast_q31() 365 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_correlate_fast_q31() 372 x0 = x1; in arm_correlate_fast_q31() 373 x1 = x2; in arm_correlate_fast_q31()
|
D | arm_conv_partial_fast_q31.c | 79 q31_t x0, x1, x2, x3, c0; in arm_conv_partial_fast_q31() local 284 x1 = *px++; in arm_conv_partial_fast_q31() 303 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_partial_fast_q31() 316 acc0 = (q31_t) ((((q63_t) acc0 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_partial_fast_q31() 327 x1 = *px++; in arm_conv_partial_fast_q31() 337 acc3 = (q31_t) ((((q63_t) acc3 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_partial_fast_q31() 350 acc2 = (q31_t) ((((q63_t) acc2 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_partial_fast_q31() 371 acc1 = (q31_t) ((((q63_t) acc1 << 32) + ((q63_t) x1 * c0)) >> 32); in arm_conv_partial_fast_q31() 378 x0 = x1; in arm_conv_partial_fast_q31() 379 x1 = x2; in arm_conv_partial_fast_q31()
|
D | arm_conv_fast_q15.c | 76 …q31_t x0, x1, x2, x3, c0; /* Temporary variables to hold state and coefficien… in arm_conv_fast_q15() local 286 x1 = read_q15x2 ((q15_t *) px + 1); in arm_conv_fast_q15() 304 acc1 = __SMLADX(x1, c0, acc1); in arm_conv_fast_q15() 331 x1 = read_q15x2 ((q15_t *) px + 3); in arm_conv_fast_q15() 338 acc3 = __SMLADX(x1, c0, acc3); in arm_conv_fast_q15() 366 acc1 = __SMLAD(x1, c0, acc1); in arm_conv_fast_q15() 367 acc2 = __SMLADX(x1, c0, acc2); in arm_conv_fast_q15() 385 acc1 = __SMLADX(x1, c0, acc1); in arm_conv_fast_q15() 403 acc1 = __SMLADX(x1, c0, acc1); in arm_conv_fast_q15() 420 acc0 = __SMLADX(x1, c0, acc0); in arm_conv_fast_q15()
|
/cmsis-dsp-latest/Source/InterpolationFunctions/ |
D | arm_linear_interp_f32.c | 84 float32_t x0, x1; /* Nearest input values */ in arm_linear_interp_f32() local 91 i = (int32_t) ((x - S->x1) / xSpacing); in arm_linear_interp_f32() 93 if (x < S->x1) in arm_linear_interp_f32() 106 x0 = S->x1 + i * xSpacing; in arm_linear_interp_f32() 107 x1 = S->x1 + (i + 1) * xSpacing; in arm_linear_interp_f32() 114 y = y0 + (x - x0) * ((y1 - y0) / (x1 - x0)); in arm_linear_interp_f32()
|
D | arm_linear_interp_f16.c | 56 float16_t x0, x1; /* Nearest input values */ in arm_linear_interp_f16() local 63 i = (int32_t) (((_Float16)x - (_Float16)S->x1) / (_Float16)xSpacing); in arm_linear_interp_f16() 65 if (((_Float16)x < (_Float16)S->x1)) in arm_linear_interp_f16() 78 x0 = (_Float16)S->x1 + (_Float16)i * (_Float16)xSpacing; in arm_linear_interp_f16() 79 x1 = (_Float16)S->x1 + (_Float16)(i + 1) * (_Float16)xSpacing; in arm_linear_interp_f16() 87 (((_Float16)y1 - (_Float16)y0) / ((_Float16)x1 - (_Float16)x0)); in arm_linear_interp_f16()
|