/cmsis-dsp-latest/Source/SupportFunctions/ |
D | arm_bitonic_sort_f32.c | 210 float32x4x2_t out1 = vzipq_f32(a.val[0], b.val[0]); in arm_bitonic_resort_16_f32() 211 float32x4x2_t out2 = vzipq_f32(a.val[1], b.val[1]); in arm_bitonic_resort_16_f32() 213 vst1q_f32(pOut, out1.val[0]); in arm_bitonic_resort_16_f32() 214 vst1q_f32(pOut+4, out1.val[1]); in arm_bitonic_resort_16_f32() 215 vst1q_f32(pOut+8, out2.val[0]); in arm_bitonic_resort_16_f32() 216 vst1q_f32(pOut+12, out2.val[1]); in arm_bitonic_resort_16_f32() 273 a = vcombine_f32(vget_low_f32(ab.val[0]), vget_low_f32(cd.val[0])); in arm_bitonic_sort_16_f32() 274 b = vcombine_f32(vget_low_f32(ab.val[1]), vget_low_f32(cd.val[1])); in arm_bitonic_sort_16_f32() 275 c = vcombine_f32(vget_high_f32(ab.val[0]), vget_high_f32(cd.val[0])); in arm_bitonic_sort_16_f32() 276 d = vcombine_f32(vget_high_f32(ab.val[1]), vget_high_f32(cd.val[1])); in arm_bitonic_sort_16_f32() [all …]
|
D | arm_float_to_q7.c | 85 tmp.val[0] = vmulq(tmp.val[0], maxQ); in arm_float_to_q7() 86 tmp.val[1] = vmulq(tmp.val[1], maxQ); in arm_float_to_q7() 87 tmp.val[2] = vmulq(tmp.val[2], maxQ); in arm_float_to_q7() 88 tmp.val[3] = vmulq(tmp.val[3], maxQ); in arm_float_to_q7() 93 evVec = vqmovnbq(evVec, vcvtaq_s32_f32(tmp.val[0])); in arm_float_to_q7() 94 evVec = vqmovntq(evVec, vcvtaq_s32_f32(tmp.val[2])); in arm_float_to_q7() 98 oddVec = vqmovnbq(oddVec, vcvtaq_s32_f32(tmp.val[1])); in arm_float_to_q7() 99 oddVec = vqmovntq(oddVec, vcvtaq_s32_f32(tmp.val[3])); in arm_float_to_q7()
|
/cmsis-dsp-latest/PrivateInclude/ |
D | arm_sorting.h | 111 float32x4_t vtrn128_temp = a.val[1]; \ 112 a.val[1] = b.val[0]; \ 113 b.val[0] = vtrn128_temp ; \ 131 a_0 = vget_low_f32(a.val[0]); \ 132 a_1 = vget_high_f32(a.val[0]); \ 133 a_2 = vget_low_f32(a.val[1]); \ 134 a_3 = vget_high_f32(a.val[1]); \ 135 b_0 = vget_low_f32(b.val[0]); \ 136 b_1 = vget_high_f32(b.val[0]); \ 137 b_2 = vget_low_f32(b.val[1]); \ [all …]
|
/cmsis-dsp-latest/Source/TransformFunctions/ |
D | arm_rfft_fast_f32.c | 108 xB.val[0] = vldrwq_gather_shifted_offset_f32(pB, vecStridesBkwd); in stage_rfft_f32() 109 xB.val[1] = vldrwq_gather_shifted_offset_f32(&pB[1], vecStridesBkwd); in stage_rfft_f32() 111 xB.val[1] = vnegq_f32(xB.val[1]); in stage_rfft_f32() 119 tmp1.val[0] = vaddq_f32(xA.val[0],xB.val[0]); in stage_rfft_f32() 120 tmp1.val[1] = vaddq_f32(xA.val[1],xB.val[1]); in stage_rfft_f32() 122 tmp2.val[0] = vsubq_f32(xB.val[0],xA.val[0]); in stage_rfft_f32() 123 tmp2.val[1] = vsubq_f32(xB.val[1],xA.val[1]); in stage_rfft_f32() 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() [all …]
|
D | arm_rfft_fast_f16.c | 113 xB.val[0] = vldrhq_gather_shifted_offset_f16(pB, vecStridesBkwd); in stage_rfft_f16() 114 xB.val[1] = vldrhq_gather_shifted_offset_f16(&pB[1], vecStridesBkwd); in stage_rfft_f16() 116 xB.val[1] = vnegq_f16(xB.val[1]); in stage_rfft_f16() 124 tmp1.val[0] = vaddq_f16(xA.val[0],xB.val[0]); in stage_rfft_f16() 125 tmp1.val[1] = vaddq_f16(xA.val[1],xB.val[1]); in stage_rfft_f16() 127 tmp2.val[0] = vsubq_f16(xB.val[0],xA.val[0]); in stage_rfft_f16() 128 tmp2.val[1] = vsubq_f16(xB.val[1],xA.val[1]); in stage_rfft_f16() 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() [all …]
|
/cmsis-dsp-latest/Include/ |
D | arm_math_memory.h | 79 q31_t val; in read_q15x2() local 82 memcpy (&val, pQ15, 4); in read_q15x2() 84 val = (pQ15[1] << 16) | (pQ15[0] & 0x0FFFF) ; in read_q15x2() 87 return (val); in read_q15x2() 113 q31_t val = value; in write_q15x2_ia() local 115 memcpy (*pQ15, &val, 4); in write_q15x2_ia() 117 (*pQ15)[0] = (q15_t)(val & 0x0FFFF); in write_q15x2_ia() 118 (*pQ15)[1] = (q15_t)((val >> 16) & 0x0FFFF); in write_q15x2_ia() 133 q31_t val = value; in write_q15x2() local 136 memcpy (pQ15, &val, 4); in write_q15x2() [all …]
|
/cmsis-dsp-latest/dsppp/Include/dsppp/DSP/ |
D | memory.hpp | 29 int32_t val; in read_q15x2() local 33 memcpy (&val, p, 4); in read_q15x2() 35 val = (p[1] << 16) | (p[0] & 0x0FFFF) ; in read_q15x2() 38 return (val); in read_q15x2() 47 int32_t val = value; in write_q15x2() local 51 memcpy (p, &val, 4); in write_q15x2() 53 p[0] = (int16_t)(val & 0x0FFFF); in write_q15x2() 54 p[1] = (int16_t)(val >> 16); in write_q15x2() 62 int32_t val; in read_q7x4() local 66 memcpy (&val, p, 4); in read_q7x4() [all …]
|
D | q7.hpp | 26 explicit Q7DSPVector(int32_t val):v(val){}; in Q7DSPVector() 85 __STATIC_FORCEINLINE Q7DSPVector vconst(Q7 val) in vconst() argument 87 return(Q7DSPVector(__PACKq7(val.v, val.v, val.v, val.v))); in vconst() 198 inline void vstore1(Q7 *p,const Q7DSPVector val) in vstore1() argument 200 write_q7x4 (p, val.v); in vstore1() 205 inline void vstore1(Q7 *p,const Q7DSPVector val) in vstore1() argument 207 p[0] = Q7(val.v & 0x0FF); in vstore1() 208 p[S] = Q7(val.v >> 8); in vstore1() 209 p[2*S] = Q7(val.v >> 16); in vstore1() 210 p[3*S] = Q7(val.v >> 24); in vstore1() [all …]
|
D | q15.hpp | 37 explicit Q15DSPVector(int32_t val):v(val){}; in Q15DSPVector() 149 __STATIC_FORCEINLINE Q15DSPVector vconst(Q15 val) in vconst() argument 151 return(Q15DSPVector(__PKHBT(val.v, val.v, 16))); in vconst() 254 inline void vstore1(Q15 *p,const Q15DSPVector val) in vstore1() argument 256 write_q15x2 (p, val.v); in vstore1() 261 inline void vstore1(Q15 *p,const Q15DSPVector val) in vstore1() argument 263 p[0] = Q15(val.v & 0x0FFFF); in vstore1() 264 p[S] = Q15(val.v >> 16); in vstore1() 269 const Q15DSPVector val) in vstore1() argument 271 p[0] = Q15(val.v & 0x0FFFF); in vstore1() [all …]
|
/cmsis-dsp-latest/Source/ComplexMathFunctions/ |
D | arm_cmplx_mag_squared_f32.c | 89 sum = vmulq(vecSrc.val[0], vecSrc.val[0]); in arm_cmplx_mag_squared_f32() 90 sum = vfmaq(sum, vecSrc.val[1], vecSrc.val[1]); in arm_cmplx_mag_squared_f32() 150 vRealA = vmulq_f32(vecA.val[0], vecA.val[0]); in arm_cmplx_mag_squared_f32() 151 vImagA = vmulq_f32(vecA.val[1], vecA.val[1]); in arm_cmplx_mag_squared_f32() 157 vRealB = vmulq_f32(vecB.val[0], vecB.val[0]); in arm_cmplx_mag_squared_f32() 158 vImagB = vmulq_f32(vecB.val[1], vecB.val[1]); in arm_cmplx_mag_squared_f32()
|
D | arm_cmplx_mag_f32.c | 100 sum = vmulq(vecSrc.val[0], vecSrc.val[0]); in arm_cmplx_mag_f32() 101 sum = vfmaq(sum, vecSrc.val[1], vecSrc.val[1]); in arm_cmplx_mag_f32() 188 vRealA = vmulq_f32(vecA.val[0], vecA.val[0]); in arm_cmplx_mag_f32() 189 vImagA = vmulq_f32(vecA.val[1], vecA.val[1]); in arm_cmplx_mag_f32() 192 vRealB = vmulq_f32(vecB.val[0], vecB.val[0]); in arm_cmplx_mag_f32() 193 vImagB = vmulq_f32(vecB.val[1], vecB.val[1]); in arm_cmplx_mag_f32()
|
D | arm_cmplx_mult_cmplx_f32.c | 207 outCplx.val[0] = vmulq_f32(va.val[0], vb.val[0]); in arm_cmplx_mult_cmplx_f32() 208 outCplx.val[0] = vmlsq_f32(outCplx.val[0], va.val[1], vb.val[1]); in arm_cmplx_mult_cmplx_f32() 211 outCplx.val[1] = vmulq_f32(va.val[0], vb.val[1]); in arm_cmplx_mult_cmplx_f32() 212 outCplx.val[1] = vmlaq_f32(outCplx.val[1], va.val[1], vb.val[0]); in arm_cmplx_mult_cmplx_f32()
|
D | arm_cmplx_dot_prod_f32.c | 217 accR = vmlaq_f32(accR,vec1.val[0],vec2.val[0]); in arm_cmplx_dot_prod_f32() 218 accR = vmlsq_f32(accR,vec1.val[1],vec2.val[1]); in arm_cmplx_dot_prod_f32() 221 accI = vmlaq_f32(accI,vec1.val[1],vec2.val[0]); in arm_cmplx_dot_prod_f32() 222 accI = vmlaq_f32(accI,vec1.val[0],vec2.val[1]); in arm_cmplx_dot_prod_f32() 232 accR = vmlaq_f32(accR,vec3.val[0],vec4.val[0]); in arm_cmplx_dot_prod_f32() 233 accR = vmlsq_f32(accR,vec3.val[1],vec4.val[1]); in arm_cmplx_dot_prod_f32() 236 accI = vmlaq_f32(accI,vec3.val[1],vec4.val[0]); in arm_cmplx_dot_prod_f32() 237 accI = vmlaq_f32(accI,vec3.val[0],vec4.val[1]); in arm_cmplx_dot_prod_f32()
|
D | arm_cmplx_mag_f16.c | 74 sum = vmulq(vecSrc.val[0], vecSrc.val[0]); in arm_cmplx_mag_f16() 75 sum = vfmaq(sum, vecSrc.val[1], vecSrc.val[1]); in arm_cmplx_mag_f16() 120 sum = vmulq(vecSrc.val[0], vecSrc.val[0]); in arm_cmplx_mag_f16() 121 sum = vfmaq(sum, vecSrc.val[1], vecSrc.val[1]); in arm_cmplx_mag_f16()
|
/cmsis-dsp-latest/ComputeLibrary/Include/ |
D | NEMath.h | 57 static inline float32x4_t vfloorq_f32(float32x4_t val); 126 static inline float32x4_t vtanhq_f32(float32x4_t val); 137 static inline float32x4_t vpowq_f32(float32x4_t val, float32x4_t n); 150 static inline float16x8_t vtanhq_f16(float16x8_t val); 201 static inline float16x8_t vpowq_f16(float16x8_t val, float16x8_t n); 216 static inline float32x4_t vfloorq_f32(float32x4_t val) in vfloorq_f32() argument 220 const int32x4_t z = vcvtq_s32_f32(val); in vfloorq_f32() 223 return vbslq_f32(vcgtq_f32(r, val), vsubq_f32(r, vld1q_f32(CONST_1)), r); in vfloorq_f32() 310 float32x4_t val = vmlsq_f32(x, vcvtq_f32_s32(m), vld1q_f32(CONST_LN2)); in vexpq_f32() local 313 float32x4_t poly = vtaylor_polyq_f32(val, exp_tab); in vexpq_f32() [all …]
|
/cmsis-dsp-latest/dsppp/Include/dsppp/Helium/ |
D | float.hpp | 692 inline void vstore1(float32_t *p,const float32x4_t val) in vstore1() argument 694 vst1q(p,val); in vstore1() 699 inline void vstore1(float32_t *p,const float32x4_t val) in vstore1() argument 705 vstrwq_scatter_shifted_offset_f32(p,offset,val); in vstore1() 717 inline void vstore1(float32_t *p,const index_t stride,const float32x4_t val) in vstore1() argument 721 vstrwq_scatter_shifted_offset_f32(p,offset,val); in vstore1() 738 …inline void vstore1_z(float32_t *p,const float32x4_t val,const std::size_t nb,const mve_pred16_t p… in vstore1_z() argument 741 vstrwq_p(p,val,p0); in vstore1_z() 746 …inline void vstore1_z(float32_t *p,const float32x4_t val,const std::size_t nb,const mve_pred16_t p… in vstore1_z() argument 753 vstrwq_scatter_shifted_offset_p_f32(p,offset,val,p0); in vstore1_z() [all …]
|
D | q15.hpp | 109 __STATIC_FORCEINLINE int16x8_t vconst(Q15 val) in vconst() argument 111 return(vdupq_n_s16(val.v)); in vconst() 114 __STATIC_FORCEINLINE int16x8_t vconst_tail(Q15 val, in vconst_tail() argument 117 return(vdupq_x_n_s16(val.v,p0)); in vconst_tail() 386 inline void vstore1(Q15 *p,const int16x8_t val) in vstore1() argument 388 vst1q(reinterpret_cast<int16_t*>(p),val); in vstore1() 393 inline void vstore1(Q15 *p,const int16x8_t val) in vstore1() argument 399 return(vstrhq_scatter_shifted_offset_s16(reinterpret_cast<int16_t*>(p),offset,val)); in vstore1() 404 inline void vstore1(Q15 *p,const int16x8_t val) in vstore1() argument 408 *p = Q15(val[i]); in vstore1() [all …]
|
D | q7.hpp | 72 __STATIC_FORCEINLINE int8x16_t vconst(Q7 val) in vconst() argument 74 return(vdupq_n_s8(val.v)); in vconst() 77 __STATIC_FORCEINLINE int8x16_t vconst_tail(Q7 val, in vconst_tail() argument 80 return(vdupq_x_n_s8(val.v,p0)); in vconst_tail() 329 inline void vstore1(Q7 *p,const int8x16_t val) in vstore1() argument 331 vst1q(reinterpret_cast<int8_t*>(p),val); in vstore1() 336 inline void vstore1(Q7 *p,const int8x16_t val) in vstore1() argument 343 return(vstrbq_scatter_offset_s8(reinterpret_cast<int8_t*>(p),offset,val)); in vstore1() 348 inline void vstore1(Q7 *p,const int8x16_t val) in vstore1() argument 352 *p = Q7(val[i]); in vstore1() [all …]
|
D | q31.hpp | 72 __STATIC_FORCEINLINE int32x4_t vconst(Q31 val) in vconst() argument 74 return(vdupq_n_s32(val.v)); in vconst() 77 __STATIC_FORCEINLINE int32x4_t vconst_tail(Q31 val, in vconst_tail() argument 80 return(vdupq_x_n_s32(val.v,p0)); in vconst_tail() 256 inline void vstore1(Q31 *p,const int32x4_t val) in vstore1() argument 258 vst1q(reinterpret_cast<int32_t*>(p),val); in vstore1() 263 inline void vstore1(Q31 *p,const int32x4_t val) in vstore1() argument 267 return(vstrwq_scatter_shifted_offset_s32(reinterpret_cast<int32_t*>(p),offset,val)); in vstore1() 273 inline void vstore1(Q31 *p,const index_t stride,const int32x4_t val) in vstore1() argument 278 return(vstrwq_scatter_shifted_offset_s32(reinterpret_cast<int32_t*>(p),offset,val)); in vstore1() [all …]
|
D | half.hpp | 536 inline void vstore1(float16_t *p,const float16x8_t val) in vstore1() argument 538 vst1q(p,val); in vstore1() 543 inline void vstore1(float16_t *p,const float16x8_t val) in vstore1() argument 546 vstrhq_scatter_shifted_offset_f16(p,offset,val); in vstore1() 551 inline void vstore1(float16_t *p,const float16x8_t val) in vstore1() argument 555 *p = val[i]; in vstore1() 564 const float16x8_t val) in vstore1() argument 570 vstrhq_scatter_shifted_offset_f16(p,offset,val); in vstore1() 576 *p = val[i]; in vstore1() 585 const float16x8_t val, in vstore1_z() argument [all …]
|
/cmsis-dsp-latest/Scripts/ |
D | genMVETwiddleCoefs.py | 43 val = "%d," % d 44 nb = nb + len(val) 47 nb = len(val) 48 print(val,end="",file=f) 57 val = "%.20ff," % f32(d) 58 nb = nb + len(val) 61 nb = len(val) 62 print(val,end="",file=f) 71 val = "(float16_t)%.13ff," % f16(d) 72 nb = nb + len(val) [all …]
|
/cmsis-dsp-latest/dsppp/Include/dsppp/Neon/ |
D | float.hpp | 79 inline void vstore1(float32_t *p,const float32x4_t val) in vstore1() argument 81 return(vst1q(p,val)); in vstore1() 86 inline void vstore1(float32_t *p,const float32x4_t val) in vstore1() argument 88 *p = val[0]; in vstore1() 91 *p = val[1]; in vstore1() 94 *p = val[2]; in vstore1() 97 *p = val[3]; in vstore1()
|
/cmsis-dsp-latest/Testing/FrameworkSource/ |
D | Semihosting.cpp | 514 uint32_t val; in ImportParams() local 540 fscanf(params,"%d\n",&val); in ImportParams() 541 *p++ = val; in ImportParams() 599 uint64_t val; in ImportPattern_f64() local 622 fscanf(pattern,"0x%16llx\n",&val); in ImportPattern_f64() 623 *ptr = TOTYP(float64_t,val); in ImportPattern_f64() 638 uint32_t val; in ImportPattern_f32() local 662 fscanf(pattern,"0x%08X\n",&val); in ImportPattern_f32() 664 *ptr = TOTYP(float32_t,val); in ImportPattern_f32() 680 uint32_t val; in ImportPattern_f16() local [all …]
|
/cmsis-dsp-latest/Documentation/Doxygen/style_template/ |
D | resize.js | 34 var val = localStorage.getItem(cookie_namespace+'_width'); 35 if (val) return val; 46 var val = document.cookie.substring(valStart, valEnd); 47 return val; 54 function writeSetting(cookie, val) argument 57 localStorage.setItem(cookie_namespace+"_width",val); 62 …document.cookie = cookie_namespace + "_" + cookie + "=" + val + "; SameSite=Lax; expires=" + expir…
|
/cmsis-dsp-latest/Testing/Source/Tests/ |
D | FastMathQ63.cpp | 28 int32_t val; in test_norm_64_to_32u() local 31 arm_norm_64_to_32u(inp[i],&val,&norm); in test_norm_64_to_32u() 32 outValp[i]=val; in test_norm_64_to_32u() 51 int32_t val; in test_div_int64_to_int32() local 53 val = arm_div_int64_to_int32(denp[i],nump[i]); in test_div_int64_to_int32() 54 outValp[i]=val; in test_div_int64_to_int32()
|