Home
last modified time | relevance | path

Searched refs:w (Results 1 – 25 of 64) sorted by relevance

123

/hal_nxp-latest/mcux/mcux-sdk/middleware/mmcau/asm-cm0p/src/
Dmmcau_sha1_functions.s113 # #24-#340 | w[i]
173 # w[i] = byterev(msg_data[k]); // w[i] = m[k]
176 # *(MMCAU_PPB_INDIRECT + (ADR+CAA)) = w[i++]; // + w[i]
194 rev r1, r1 @ w[0]
196 str r1, [sp, #0<<2+24] @ store w[0]
197 add r1, r7 @ w[0] + k[0]
202 rev r1, r1 @ w[1]
204 str r1, [sp, #1<<2+24] @ store w[1]
205 add r1, r7 @ w[1] + k[0]
210 rev r1, r1 @ w[2]
[all …]
Dmmcau_sha256_functions.s121 # #64-#252 | w[i] in loop
122 # #0-#60 | w[0-15] in next_blk
184 # w[i] = byterev(input[i]); // copy m[i] to w[i]
185 # *(MMCAU_PPB_INDIRECT + (LDR+CAA)) = w[i]; // +w[i]+h+SIGMA1(e)
216 rev r7, r7 @ w[0]
217 str r7, [sp, #0<<2] @ store w[0]
219 str r7, [r6] @ add w[i]
228 rev r7, r7 @ w[1]
229 str r7, [sp, #1<<2] @ store w[1]
231 str r7, [r6] @ add w[1]
[all …]
/hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/Source/MatrixFunctions/
Darm_mat_ldlt_f32.c43 for(int w=0;w < n; w+=4) \
48 tmpa=vldrwq_z_f32(&A[i*n + w],p0);\
49 tmpb=vldrwq_z_f32(&A[j*n + w],p0);\
51 vstrwq_p(&A[i*n + w], tmpb, p0); \
52 vstrwq_p(&A[j*n + w], tmpa, p0); \
60 for(int w=0;w < n; w++) \
63 tmp = A[w*n + i]; \
64 A[w*n + i] = A[w*n + j];\
65 A[w*n + j] = tmp; \
180 int w; in arm_mat_ldlt_f32() local
[all …]
Darm_mat_ldlt_f64.c36 for(int w=0;w < n; w++) \
39 tmp = A[i*n + w]; \
40 A[i*n + w] = A[j*n + w];\
41 A[j*n + w] = tmp; \
45 for(int w=0;w < n; w++) \
48 tmp = A[w*n + i]; \
49 A[w*n + i] = A[w*n + j];\
50 A[w*n + j] = tmp; \
151 for(int w=k+1;w<n;w++) in arm_mat_ldlt_f64() local
155 pA[w*n+x] = pA[w*n+x] - pA[w*n+k] * pA[x*n+k] / a; in arm_mat_ldlt_f64()
[all …]
/hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/Source/FilteringFunctions/
Darm_lms_norm_f32.c177 …float32_t w, x0, in; /* weight factor, temporary variable to hold input … in arm_lms_norm_f32() local
185 w = 0.0f; in arm_lms_norm_f32()
260 w = (e * mu) / (energy + 0.000000119209289f); in arm_lms_norm_f32()
278 bV = vmlaq_n_f32(bV,xV,w); in arm_lms_norm_f32()
294 *pb += w * (*px++); in arm_lms_norm_f32()
363 float32_t w; /* Weight factor */ in arm_lms_norm_f32() local
371 w = 0.0f; in arm_lms_norm_f32()
452 w = (e * mu) / (energy + 0.000000119209289f); in arm_lms_norm_f32()
469 *pb += w * (*px++); in arm_lms_norm_f32()
472 *pb += w * (*px++); in arm_lms_norm_f32()
[all …]
Darm_lms_f32.c182 float32_t w = 0.0f; /* weight factor */ in arm_lms_f32() local
252 w = e * mu; in arm_lms_f32()
270 bV = vmlaq_n_f32(bV,xV,w); in arm_lms_f32()
286 *pb = *pb + (w * (*px++)); in arm_lms_f32()
352 float32_t w; /* Weight factor */ in arm_lms_f32() local
358 w = 0.0f; in arm_lms_f32()
428 w = e * mu; in arm_lms_f32()
446 *pb += w * (*px++); in arm_lms_f32()
449 *pb += w * (*px++); in arm_lms_f32()
452 *pb += w * (*px++); in arm_lms_f32()
[all …]
Darm_lms_norm_q15.c83 q15_t w = 0, in; /* Weight factor and state */ in arm_lms_norm_q15() local
188 w = (q15_t) __SSAT((q31_t) acc, 16); in arm_lms_norm_q15()
204 coef = (q31_t) *pb + (((q31_t) w * (*px++)) >> 15); in arm_lms_norm_q15()
207 coef = (q31_t) *pb + (((q31_t) w * (*px++)) >> 15); in arm_lms_norm_q15()
210 coef = (q31_t) *pb + (((q31_t) w * (*px++)) >> 15); in arm_lms_norm_q15()
213 coef = (q31_t) *pb + (((q31_t) w * (*px++)) >> 15); in arm_lms_norm_q15()
233 coef = (q31_t) *pb + (((q31_t) w * (*px++)) >> 15); in arm_lms_norm_q15()
Darm_lms_norm_q31.c83 q31_t w = 0, in; /* Weight factor and state */ in arm_lms_norm_q31() local
189 w = clip_q63_to_q31(((q63_t) errorXmu * oneByEnergy) >> (31 - postShift)); in arm_lms_norm_q31()
208 coef = (q31_t) (((q63_t) w * (*px++)) >> (32)); in arm_lms_norm_q31()
214 coef = (q31_t) (((q63_t) w * (*px++)) >> (32)); in arm_lms_norm_q31()
218 coef = (q31_t) (((q63_t) w * (*px++)) >> (32)); in arm_lms_norm_q31()
222 coef = (q31_t) (((q63_t) w * (*px++)) >> (32)); in arm_lms_norm_q31()
243 coef = (q31_t) (((q63_t) w * (*px++)) >> (32)); in arm_lms_norm_q31()
/hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/Source/SupportFunctions/
Darm_barycenter_f32.c63 float32_t accum, w; in arm_barycenter_f32() local
144 w = *pW++; in arm_barycenter_f32()
145 accum += w; in arm_barycenter_f32()
152 outV = vfmaq(outV, inV, w); in arm_barycenter_f32()
163 *pOut = *pOut + *pIn++ * w; in arm_barycenter_f32()
205 float32_t accum, w,w1,w2,w3,w4; in arm_barycenter_f32() local
301 w = *pW++; in arm_barycenter_f32()
302 accum += w; in arm_barycenter_f32()
309 outV = vmlaq_n_f32(outV,inV,w); in arm_barycenter_f32()
320 *pOut = *pOut + *pIn++ * w; in arm_barycenter_f32()
[all …]
Darm_barycenter_f16.c77 float16_t accum, w; in arm_barycenter_f16() local
158 w = *pW++; in arm_barycenter_f16()
159 accum += w; in arm_barycenter_f16()
166 outV = vfmaq(outV, inV, w); in arm_barycenter_f16()
177 *pOut = *pOut + *pIn++ * w; in arm_barycenter_f16()
216 float16_t accum, w; in arm_barycenter_f16() local
241 w = *pW++; in arm_barycenter_f16()
242 accum += w; in arm_barycenter_f16()
247 *pOut = *pOut + *pIn++ * w; in arm_barycenter_f16()
/hal_nxp-latest/mcux/mcux-sdk/CMSIS/NN/Source/ConvolutionFunctions/
Darm_convolve_wrapper_s8.c62 … if ((conv_params->padding.w == 0) && (conv_params->padding.h == 0) && (input_dims->c % 4 == 0) && in arm_convolve_wrapper_s8()
63 …(conv_params->stride.w == 1) && (conv_params->stride.h == 1) && (filter_dims->w == 1) && (filter_d… in arm_convolve_wrapper_s8()
77 …tput_dims->h == 1) && (input_dims->h == 1) && (filter_dims->h == 1) && (output_dims->w % 4 == 0) && in arm_convolve_wrapper_s8()
113 … if ((conv_params->padding.w == 0) && (conv_params->padding.h == 0) && (input_dims->c % 4 == 0) && in arm_convolve_wrapper_s8_get_buffer_size()
114 …(conv_params->stride.w == 1) && (conv_params->stride.h == 1) && (filter_dims->w == 1) && (filter_d… in arm_convolve_wrapper_s8_get_buffer_size()
118 …tput_dims->h == 1) && (input_dims->h == 1) && (filter_dims->h == 1) && (output_dims->w % 4 == 0) && in arm_convolve_wrapper_s8_get_buffer_size()
Darm_depthwise_conv_s8.c248 input_dims->w, in arm_depthwise_conv_s8()
254 filter_dims->w, in arm_depthwise_conv_s8()
256 dw_conv_params->padding.w, in arm_depthwise_conv_s8()
258 dw_conv_params->stride.w, in arm_depthwise_conv_s8()
264 output_dims->w, in arm_depthwise_conv_s8()
275 input_dims->w, in arm_depthwise_conv_s8()
281 filter_dims->w, in arm_depthwise_conv_s8()
283 dw_conv_params->padding.w, in arm_depthwise_conv_s8()
285 dw_conv_params->stride.w, in arm_depthwise_conv_s8()
291 output_dims->w, in arm_depthwise_conv_s8()
Darm_convolve_1_x_n_s8.c64 if (output_dims->w % 4 != 0) in arm_convolve_1_x_n_s8()
73 const uint16_t input_x = input_dims->w; in arm_convolve_1_x_n_s8()
74 const uint16_t kernel_x = filter_dims->w; in arm_convolve_1_x_n_s8()
75 const uint16_t output_x = output_dims->w; in arm_convolve_1_x_n_s8()
78 const uint16_t pad_x = conv_params->padding.w; in arm_convolve_1_x_n_s8()
79 const uint16_t stride_x = conv_params->stride.w; in arm_convolve_1_x_n_s8()
193 return (2 * input_dims->c * filter_dims->w * filter_dims->h) * sizeof(int16_t); in arm_convolve_1_x_n_s8_get_buffer_size()
Darm_depthwise_conv_s8_opt.c73 const int32_t input_x = input_dims->w; in arm_depthwise_conv_s8_opt()
75 const int32_t kernel_x = filter_dims->w; in arm_depthwise_conv_s8_opt()
77 const int32_t pad_x = dw_conv_params->padding.w; in arm_depthwise_conv_s8_opt()
79 const int32_t stride_x = dw_conv_params->stride.w; in arm_depthwise_conv_s8_opt()
83 const int32_t output_x = output_dims->w; in arm_depthwise_conv_s8_opt()
416 return (2 * input_dims->c * filter_dims->w * filter_dims->h) * (int32_t)sizeof(int16_t) + 4; in arm_depthwise_conv_s8_opt_get_buffer_size()
418 return (input_dims->c * filter_dims->w * filter_dims->h) * sizeof(int16_t); in arm_depthwise_conv_s8_opt_get_buffer_size()
Darm_convolve_s8.c67 const uint16_t input_x = input_dims->w; in arm_convolve_s8()
70 const uint16_t kernel_x = filter_dims->w; in arm_convolve_s8()
72 const uint16_t output_x = output_dims->w; in arm_convolve_s8()
76 const uint16_t pad_x = conv_params->padding.w; in arm_convolve_s8()
78 const uint16_t stride_x = conv_params->stride.w; in arm_convolve_s8()
370 return (2 * input_dims->c * filter_dims->w * filter_dims->h) * (int32_t)sizeof(int16_t); in arm_convolve_s8_get_buffer_size()
Darm_depthwise_conv_3x3_s8.c67 const int32_t input_x = input_dims->w; in arm_depthwise_conv_3x3_s8()
71 const int32_t pad_x = dw_conv_params->padding.w; in arm_depthwise_conv_3x3_s8()
73 const int32_t stride_x = dw_conv_params->stride.w; in arm_depthwise_conv_3x3_s8()
77 const int32_t output_x = output_dims->w; in arm_depthwise_conv_3x3_s8()
90 if (pad_x > 1 || filter_dims->w != 3 || filter_dims->h != 3) in arm_depthwise_conv_3x3_s8()
Darm_convolve_1x1_s8_fast.c65 if (input_dims->c % 4 != 0 || conv_params->padding.w != 0 || conv_params->padding.h != 0 || in arm_convolve_1x1_s8_fast()
66 conv_params->stride.w != 1 || conv_params->stride.h != 1) in arm_convolve_1x1_s8_fast()
77 const int32_t col_len = input_dims->w * input_dims->h * input_dims->n; in arm_convolve_1x1_s8_fast()
149 const int32_t lhs_rows = input_dims->w * input_dims->h * input_dims->n; in arm_convolve_1x1_s8_fast()
/hal_nxp-latest/mcux/mcux-sdk/CMSIS/NN/Source/PoolingFunctions/
Darm_avgpool_s8.c84 const int32_t input_x = input_dims->w; in arm_avgpool_s8()
86 const int32_t output_x = output_dims->w; in arm_avgpool_s8()
88 const int32_t stride_x = pool_params->stride.w; in arm_avgpool_s8()
90 const int32_t kernel_x = filter_dims->w; in arm_avgpool_s8()
92 const int32_t pad_x = pool_params->padding.w; in arm_avgpool_s8()
252 const int32_t input_x = input_dims->w; in arm_avgpool_s8()
254 const int32_t output_x = output_dims->w; in arm_avgpool_s8()
256 const int32_t stride_x = pool_params->stride.w; in arm_avgpool_s8()
258 const int32_t kernel_x = filter_dims->w; in arm_avgpool_s8()
260 const int32_t pad_x = pool_params->padding.w; in arm_avgpool_s8()
Darm_max_pool_s8.c171 const int32_t input_x = input_dims->w; in arm_max_pool_s8()
173 const int32_t output_x = output_dims->w; in arm_max_pool_s8()
175 const int32_t stride_x = pool_params->stride.w; in arm_max_pool_s8()
177 const int32_t kernel_x = filter_dims->w; in arm_max_pool_s8()
179 const int32_t pad_x = pool_params->padding.w; in arm_max_pool_s8()
/hal_nxp-latest/mcux/mcux-sdk/drivers/sha/
Dfsl_sha.c39 uint32_t w[SHA_BLOCK_SIZE / 4]; /*!< array of 32-bit words */ member
434 lastBlock.w[SHA_BLOCK_SIZE / 4U - 1U] = swap_bytes(8u * ctxInternal->fullMessageSize); in sha_finalize()
453 lastBlock.w[SHA_BLOCK_SIZE / 4U - 1U] = swap_bytes(8u * ctxInternal->fullMessageSize); in sha_finalize()
519 j = (sizeof(ctxInternal->blk.w) / sizeof(ctxInternal->blk.w[0])); in SHA_Init()
522 ctxInternal->blk.w[0] = 0u; in SHA_Init()
/hal_nxp-latest/mcux/mcux-sdk/CMSIS/Include/
Dcore_cm0.h209 uint32_t w; /*!< Type used for word access */ member
236 uint32_t w; /*!< Type used for word access */ member
260 uint32_t w; /*!< Type used for word access */ member
294 uint32_t w; /*!< Type used for word access */ member
Dcore_cm1.h209 uint32_t w; /*!< Type used for word access */ member
236 uint32_t w; /*!< Type used for word access */ member
260 uint32_t w; /*!< Type used for word access */ member
294 uint32_t w; /*!< Type used for word access */ member
Dcore_sc000.h215 uint32_t w; /*!< Type used for word access */ member
242 uint32_t w; /*!< Type used for word access */ member
266 uint32_t w; /*!< Type used for word access */ member
300 uint32_t w; /*!< Type used for word access */ member
Dcore_cm0plus.h220 uint32_t w; /*!< Type used for word access */ member
247 uint32_t w; /*!< Type used for word access */ member
271 uint32_t w; /*!< Type used for word access */ member
305 uint32_t w; /*!< Type used for word access */ member
/hal_nxp-latest/mcux/mcux-sdk/drivers/cau3/
Dfsl_cau3.c98 uint32_t w[CAU3_HASH_BLOCK_SIZE / 4]; /*!< array of 32-bit words */ member
123 uint32_t w[64 / 4]; /*!< array of 32-bit words */ member
2011 lastBlock.w[15] = __REV(8u * ctxInternal->fullMessageSize); in cau3_hash_finalize()
2038 lastBlock.w[15] = __REV(8u * ctxInternal->fullMessageSize); in cau3_hash_finalize()
2080 j = sizeof(ctxInternal->blk.w) / sizeof(ctxInternal->blk.w[0]); in CAU3_HASH_Init()
2083 ctxInternal->blk.w[0] = 0u; in CAU3_HASH_Init()
4516 uint32_t w[8]; in CAU3_CHACHA20_POLY1305_SetKey() member
4519 for (uint32_t i = 0; i < ARRAY_SIZE(tempKey.w); i++) in CAU3_CHACHA20_POLY1305_SetKey()
4521 tempKey.w[i] = __REV(((const uint32_t *)(uintptr_t)key)[i]); in CAU3_CHACHA20_POLY1305_SetKey()
4532 uint32_t w[4]; in cau3_load_nonce() member
[all …]

123