| /hal_nxp-latest/mcux/middleware/wifi_nxp/sdio_nxp_abs/incl/ |
| D | mlan_sdio.h | 31 #define MP_TX_AGGR_IN_PROGRESS(a) (a->mpa_tx.pkt_cnt > 0) argument
34 #define MP_TX_AGGR_BUF_HAS_ROOM(a, mbuf, len) ((a->mpa_tx.buf_len + len) <= a->mpa_tx.buf_size) argument
37 #define MP_TX_AGGR_BUF_PUT(a, mbuf, port) \ argument
40 pmadapter->callbacks.moal_memmove(a->pmoal_handle, &a->mpa_tx.buf[a->mpa_tx.buf_len], \
42 a->mpa_tx.buf_len += mbuf->data_len; \
43 if (!a->mpa_tx.pkt_cnt) \
45 a->mpa_tx.start_port = port; \
47 if (a->mpa_tx.start_port <= port) \
49 a->mpa_tx.ports |= (1 << (a->mpa_tx.pkt_cnt)); \
53 a->mpa_tx.ports |= (1 << (a->mpa_tx.pkt_cnt + 1 + (MAX_PORT - a->mp_end_port))); \
[all …]
|
| /hal_nxp-latest/mcux/middleware/mcux-sdk-middleware-connectivity-framework/platform/rw61x/configs/ |
| D | fwk_lfs_config.h | 53 static inline uint32_t lfs_max(uint32_t a, uint32_t b) in lfs_max() argument
55 return (a > b) ? a : b; in lfs_max()
58 static inline uint32_t lfs_min(uint32_t a, uint32_t b) in lfs_min() argument
60 return (a < b) ? a : b; in lfs_min()
64 static inline uint32_t lfs_aligndown(uint32_t a, uint32_t alignment) in lfs_aligndown() argument
66 return a - (a % alignment); in lfs_aligndown()
69 static inline uint32_t lfs_alignup(uint32_t a, uint32_t alignment) in lfs_alignup() argument
71 return lfs_aligndown(a + alignment - 1, alignment); in lfs_alignup()
75 static inline uint32_t lfs_npw2(uint32_t a) in lfs_npw2() argument
78 return (32u - HAL_CLZ(a - 1)); in lfs_npw2()
[all …]
|
| /hal_nxp-latest/mcux/middleware/mcux-sdk-middleware-connectivity-framework/platform/imx_rt/configs/ |
| D | fwk_lfs_config.h | 52 static inline uint32_t lfs_max(uint32_t a, uint32_t b) in lfs_max() argument
54 return (a > b) ? a : b; in lfs_max()
57 static inline uint32_t lfs_min(uint32_t a, uint32_t b) in lfs_min() argument
59 return (a < b) ? a : b; in lfs_min()
63 static inline uint32_t lfs_aligndown(uint32_t a, uint32_t alignment) in lfs_aligndown() argument
65 return a - (a % alignment); in lfs_aligndown()
68 static inline uint32_t lfs_alignup(uint32_t a, uint32_t alignment) in lfs_alignup() argument
70 return lfs_aligndown(a + alignment - 1, alignment); in lfs_alignup()
74 static inline uint32_t lfs_npw2(uint32_t a) in lfs_npw2() argument
77 return 32 - __builtin_clz(a - 1); in lfs_npw2()
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/middleware/mmcau/asm-cm0p/src/ |
| D | mmcau_md5_functions.s | 35 # *md5_state pointer to 128-bit block of md5 state variables: a,b,c,d
86 # *md5_state pointer to 128-bit block of MD5 state variables: a,b,c,d
135 # r1 | a / num_blks (arg1)
150 add r1, r5 @ a += F(b,c,d)
152 add r1, r6 @ a += msg_data[0]
154 add r1, r5 @ a += md5_t[0]
156 rors r1, r6 @ ROTL(a,7)
157 add r1, r2 @ a = b + ROTL(a,7)
159 mov r5, r1 @ a
160 mvns r6, r1 @ ~a
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/PrivateInclude/ |
| D | arm_sorting.h | 109 #define vtrn256_128q(a, b) \ argument
111 float32x4_t vtrn128_temp = a.val[1]; \
112 a.val[1] = b.val[0]; \
116 #define vtrn128_64q(a, b) \ argument
119 ab = vget_low_f32(a); \
121 cd = vget_high_f32(a); \
123 a = vcombine_f32(ab, ef); \
127 #define vtrn256_64q(a, b) \ argument
131 a_0 = vget_low_f32(a.val[0]); \
132 a_1 = vget_high_f32(a.val[0]); \
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/Source/DistanceFunctions/ |
| D | arm_canberra_distance_f32.c | 64 f32x4_t a, b, c, accumV; in arm_canberra_distance_f32() local
70 a = vld1q(pA); in arm_canberra_distance_f32()
73 c = vabdq(a, b); in arm_canberra_distance_f32()
75 a = vabsq(a); in arm_canberra_distance_f32()
77 a = vaddq(a, b); in arm_canberra_distance_f32()
82 a = vrecip_medprec_f32(a); in arm_canberra_distance_f32()
88 a = vdupq_m_n_f32(a, 0.0f, vcmpeqq(a, 0.0f)); in arm_canberra_distance_f32()
89 c = vmulq(c, a); in arm_canberra_distance_f32()
101 a = vldrwq_z_f32(pA, p0); in arm_canberra_distance_f32()
104 c = vabdq(a, b); in arm_canberra_distance_f32()
[all …]
|
| D | arm_canberra_distance_f16.c | 77 f16x8_t a, b, c, accumV; in arm_canberra_distance_f16() local
83 a = vld1q(pA); in arm_canberra_distance_f16()
86 c = vabdq(a, b); in arm_canberra_distance_f16()
88 a = vabsq(a); in arm_canberra_distance_f16()
90 a = vaddq(a, b); in arm_canberra_distance_f16()
95 a = vrecip_hiprec_f16(a); in arm_canberra_distance_f16()
101 a = vdupq_m_n_f16(a, 0.0f, vcmpeqq(a, 0.0f)); in arm_canberra_distance_f16()
102 c = vmulq(c, a); in arm_canberra_distance_f16()
114 a = vldrhq_z_f16(pA, p0); in arm_canberra_distance_f16()
117 c = vabdq(a, b); in arm_canberra_distance_f16()
[all …]
|
| D | arm_boolean_distance_template.h | 101 uint32_t a, b, ba, bb; in FUNC() local
148 a = *pA++; in FUNC()
153 ba = a & 1; in FUNC()
155 a = a >> 1; in FUNC()
176 a = *pA++; in FUNC()
179 a = a >> (32 - blkCnt); in FUNC()
184 ba = a & 1; in FUNC()
186 a = a >> 1; in FUNC()
252 uint32_t a,b,ba,bb; in FUNC() local
370 a = *pA++; in FUNC()
[all …]
|
| D | arm_jensenshannon_distance_f32.c | 58 f32x4_t a, b, t, tmpV, accumV; in arm_jensenshannon_distance_f32() local
64 a = vld1q(pA); in arm_jensenshannon_distance_f32()
67 t = vaddq(a, b); in arm_jensenshannon_distance_f32()
70 tmpV = vmulq(a, vrecip_medprec_f32(t)); in arm_jensenshannon_distance_f32()
72 accumV = vfmaq(accumV, a, tmpV); in arm_jensenshannon_distance_f32()
91 a = vldrwq_z_f32(pA, p0); in arm_jensenshannon_distance_f32()
94 t = vaddq(a, b); in arm_jensenshannon_distance_f32()
97 tmpV = vmulq_f32(a, vrecip_medprec_f32(t)); in arm_jensenshannon_distance_f32()
99 accumV = vfmaq_m_f32(accumV, a, tmpV, p0); in arm_jensenshannon_distance_f32()
141 float32_t accum, result, tmp,a,b; in arm_jensenshannon_distance_f32() local
[all …]
|
| D | arm_euclidean_distance_f32.c | 58 f32x4_t a, b, accumV, tempV; in arm_euclidean_distance_f32() local
64 a = vld1q(pA); in arm_euclidean_distance_f32()
67 tempV = vsubq(a, b); in arm_euclidean_distance_f32()
83 a = vldrwq_z_f32(pA, p0); in arm_euclidean_distance_f32()
86 tempV = vsubq(a, b); in arm_euclidean_distance_f32()
102 float32x4_t a,b,accumV; in arm_euclidean_distance_f32() local
109 a = vld1q_f32(pA); in arm_euclidean_distance_f32()
112 a = vsubq_f32(a,b); in arm_euclidean_distance_f32()
113 accumV = vmlaq_f32(accumV,a,a); in arm_euclidean_distance_f32()
|
| D | arm_braycurtis_distance_f32.c | 58 f32x4_t a, b, c, accumDiffV, accumSumV; in arm_braycurtis_distance_f32() local
66 a = vld1q(pA); in arm_braycurtis_distance_f32()
69 c = vabdq(a, b); in arm_braycurtis_distance_f32()
72 c = vaddq_f32(a, b); in arm_braycurtis_distance_f32()
85 a = vldrwq_z_f32(pA, p0); in arm_braycurtis_distance_f32()
88 c = vabdq(a, b); in arm_braycurtis_distance_f32()
91 c = vaddq_f32(a, b); in arm_braycurtis_distance_f32()
114 float32x4_t a,b,c,accumDiffV, accumSumV; in arm_braycurtis_distance_f32() local
123 a = vld1q_f32(pA); in arm_braycurtis_distance_f32()
126 c = vabdq_f32(a,b); in arm_braycurtis_distance_f32()
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/Source/FilteringFunctions/ |
| D | arm_levinson_durbin_q31.c | 39 __STATIC_FORCEINLINE q31_t mul32x16(q31_t a, q15_t b) in mul32x16() argument
41 q31_t r = ((q63_t)a * (q63_t)b) >> 15; in mul32x16()
47 __STATIC_FORCEINLINE q31_t mul32x32(q31_t a, q31_t b) in mul32x32() argument
50 q31_t r = ((q63_t)a * b) >> 31; in mul32x32()
125 q31_t *a, in arm_levinson_durbin_q31() argument
134 a[0] = divide(phi[1], phi[0]); in arm_levinson_durbin_q31()
138 e = phi[0] - mul32x32(phi[1],a[0]); in arm_levinson_durbin_q31()
157 pA = a; in arm_levinson_durbin_q31()
183 suma += ((q63_t)a[i] * phi[p - i]); in arm_levinson_durbin_q31()
184 sumb += ((q63_t)a[i] * phi[i + 1]); in arm_levinson_durbin_q31()
[all …]
|
| D | arm_levinson_durbin_f32.c | 65 float32_t *a, in arm_levinson_durbin_f32() argument
72 a[0] = phi[1] / phi[0]; in arm_levinson_durbin_f32()
74 e = phi[0] - phi[1] * a[0]; in arm_levinson_durbin_f32()
93 pA = a; in arm_levinson_durbin_f32()
122 suma += a[i] * phi[p - i]; in arm_levinson_durbin_f32()
123 sumb += a[i] * phi[i + 1]; in arm_levinson_durbin_f32()
162 vecA = vldrwq_gather_shifted_offset_f32(a,offset); in arm_levinson_durbin_f32()
172 vstrwq_scatter_shifted_offset_f32(a, offset, tmp); in arm_levinson_durbin_f32()
185 x = a[j] - k * a[p-1-j]; in arm_levinson_durbin_f32()
186 y = a[p-1-j] - k * a[j]; in arm_levinson_durbin_f32()
[all …]
|
| D | arm_levinson_durbin_f16.c | 65 float16_t *a, in arm_levinson_durbin_f16() argument
72 a[0] = (_Float16)phi[1] / (_Float16)phi[0]; in arm_levinson_durbin_f16()
74 e = (_Float16)phi[0] - (_Float16)phi[1] * (_Float16)a[0]; in arm_levinson_durbin_f16()
93 pA = a; in arm_levinson_durbin_f16()
122 suma += (_Float16)a[i] * (_Float16)phi[p - i]; in arm_levinson_durbin_f16()
123 sumb += (_Float16)a[i] * (_Float16)phi[i + 1]; in arm_levinson_durbin_f16()
162 vecA = vldrhq_gather_shifted_offset_f16(a,offset); in arm_levinson_durbin_f16()
172 vstrhq_scatter_shifted_offset_f16(a, offset, tmp); in arm_levinson_durbin_f16()
189 x=(_Float16)a[j] - (_Float16)k * (_Float16)a[p-1-j]; in arm_levinson_durbin_f16()
190 y=(_Float16)a[p-1-j] - (_Float16)k * (_Float16)a[j]; in arm_levinson_durbin_f16()
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/Source/SupportFunctions/ |
| D | arm_bitonic_sort_f32.c | 89 static float32x4x2_t arm_bitonic_resort_8_f32(float32x4_t a, float32x4_t b, uint8_t dir) in arm_bitonic_resort_8_f32() argument
104 vtrn128_64q(a, b); in arm_bitonic_resort_8_f32()
113 vminmaxq(a, b); in arm_bitonic_resort_8_f32()
115 vminmaxq(b, a); in arm_bitonic_resort_8_f32()
117 vtrn128_32q(a, b); in arm_bitonic_resort_8_f32()
126 vminmaxq(a, b); in arm_bitonic_resort_8_f32()
128 vminmaxq(b, a); in arm_bitonic_resort_8_f32()
130 return vzipq_f32(a, b); in arm_bitonic_resort_8_f32()
134 static float32x4x2_t arm_bitonic_merge_8_f32(float32x4_t a, float32x4_t b, uint8_t dir) in arm_bitonic_merge_8_f32() argument
142 vminmaxq(a, b); in arm_bitonic_merge_8_f32()
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/Source/TransformFunctions/ |
| D | arm_bitreversal2.c | 46 uint64_t a, b, i, tmp; in arm_bitreversal_64() local
50 a = pBitRevTab[i ] >> 2; in arm_bitreversal_64()
54 tmp = pSrc[a]; in arm_bitreversal_64()
55 pSrc[a] = pSrc[b]; in arm_bitreversal_64()
59 tmp = pSrc[a+1]; in arm_bitreversal_64()
60 pSrc[a+1] = pSrc[b+1]; in arm_bitreversal_64()
80 uint32_t a, b, i, tmp; in arm_bitreversal_32() local
84 a = pBitRevTab[i ] >> 2; in arm_bitreversal_32()
88 tmp = pSrc[a]; in arm_bitreversal_32()
89 pSrc[a] = pSrc[b]; in arm_bitreversal_32()
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/Source/ComplexMathFunctions/ |
| D | arm_cmplx_mult_cmplx_f16.c | 191 _Float16 a, b, c, d; /* Temporary variables to store real and imaginary values */ in arm_cmplx_mult_cmplx_f16() local
203 a = *pSrcA++; in arm_cmplx_mult_cmplx_f16()
208 *pDst++ = (a * c) - (b * d); in arm_cmplx_mult_cmplx_f16()
209 *pDst++ = (a * d) + (b * c); in arm_cmplx_mult_cmplx_f16()
211 a = *pSrcA++; in arm_cmplx_mult_cmplx_f16()
215 *pDst++ = (a * c) - (b * d); in arm_cmplx_mult_cmplx_f16()
216 *pDst++ = (a * d) + (b * c); in arm_cmplx_mult_cmplx_f16()
218 a = *pSrcA++; in arm_cmplx_mult_cmplx_f16()
222 *pDst++ = (a * c) - (b * d); in arm_cmplx_mult_cmplx_f16()
223 *pDst++ = (a * d) + (b * c); in arm_cmplx_mult_cmplx_f16()
[all …]
|
| D | arm_cmplx_mult_cmplx_f32.c | 189 float32_t a, b, c, d; /* Temporary variables to store real and imaginary values */ in arm_cmplx_mult_cmplx_f32() local
238 a = *pSrcA++; in arm_cmplx_mult_cmplx_f32()
243 *pDst++ = (a * c) - (b * d); in arm_cmplx_mult_cmplx_f32()
244 *pDst++ = (a * d) + (b * c); in arm_cmplx_mult_cmplx_f32()
246 a = *pSrcA++; in arm_cmplx_mult_cmplx_f32()
250 *pDst++ = (a * c) - (b * d); in arm_cmplx_mult_cmplx_f32()
251 *pDst++ = (a * d) + (b * c); in arm_cmplx_mult_cmplx_f32()
253 a = *pSrcA++; in arm_cmplx_mult_cmplx_f32()
257 *pDst++ = (a * c) - (b * d); in arm_cmplx_mult_cmplx_f32()
258 *pDst++ = (a * d) + (b * c); in arm_cmplx_mult_cmplx_f32()
[all …]
|
| D | arm_cmplx_mult_cmplx_q15.c | 180 q15_t a, b, c, d; /* Temporary variables */ in arm_cmplx_mult_cmplx_q15() local
192 a = *pSrcA++; in arm_cmplx_mult_cmplx_q15()
197 *pDst++ = (q15_t) ( (((q31_t) a * c) >> 17) - (((q31_t) b * d) >> 17) ); in arm_cmplx_mult_cmplx_q15()
198 *pDst++ = (q15_t) ( (((q31_t) a * d) >> 17) + (((q31_t) b * c) >> 17) ); in arm_cmplx_mult_cmplx_q15()
200 a = *pSrcA++; in arm_cmplx_mult_cmplx_q15()
204 *pDst++ = (q15_t) ( (((q31_t) a * c) >> 17) - (((q31_t) b * d) >> 17) ); in arm_cmplx_mult_cmplx_q15()
205 *pDst++ = (q15_t) ( (((q31_t) a * d) >> 17) + (((q31_t) b * c) >> 17) ); in arm_cmplx_mult_cmplx_q15()
207 a = *pSrcA++; in arm_cmplx_mult_cmplx_q15()
211 *pDst++ = (q15_t) ( (((q31_t) a * c) >> 17) - (((q31_t) b * d) >> 17) ); in arm_cmplx_mult_cmplx_q15()
212 *pDst++ = (q15_t) ( (((q31_t) a * d) >> 17) + (((q31_t) b * c) >> 17) ); in arm_cmplx_mult_cmplx_q15()
[all …]
|
| D | arm_cmplx_mult_cmplx_q31.c | 175 q31_t a, b, c, d; /* Temporary variables */ in arm_cmplx_mult_cmplx_q31() local
187 a = *pSrcA++; in arm_cmplx_mult_cmplx_q31()
192 *pDst++ = (q31_t) ( (((q63_t) a * c) >> 33) - (((q63_t) b * d) >> 33) ); in arm_cmplx_mult_cmplx_q31()
193 *pDst++ = (q31_t) ( (((q63_t) a * d) >> 33) + (((q63_t) b * c) >> 33) ); in arm_cmplx_mult_cmplx_q31()
195 a = *pSrcA++; in arm_cmplx_mult_cmplx_q31()
199 *pDst++ = (q31_t) ( (((q63_t) a * c) >> 33) - (((q63_t) b * d) >> 33) ); in arm_cmplx_mult_cmplx_q31()
200 *pDst++ = (q31_t) ( (((q63_t) a * d) >> 33) + (((q63_t) b * c) >> 33) ); in arm_cmplx_mult_cmplx_q31()
202 a = *pSrcA++; in arm_cmplx_mult_cmplx_q31()
206 *pDst++ = (q31_t) ( (((q63_t) a * c) >> 33) - (((q63_t) b * d) >> 33) ); in arm_cmplx_mult_cmplx_q31()
207 *pDst++ = (q31_t) ( (((q63_t) a * d) >> 33) + (((q63_t) b * c) >> 33) ); in arm_cmplx_mult_cmplx_q31()
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/CMSIS/DSP/Source/MatrixFunctions/ |
| D | arm_mat_solve_lower_triangular_f32.c | 56 const arm_matrix_instance_f32 * a, in arm_mat_solve_lower_triangular_f32() argument
66 (a->numRows != a->numCols) || in arm_mat_solve_lower_triangular_f32()
67 (lt->numRows != a->numRows) ) in arm_mat_solve_lower_triangular_f32()
91 float32_t *pA = a->pData; in arm_mat_solve_lower_triangular_f32()
157 const arm_matrix_instance_f32 * a, in arm_mat_solve_lower_triangular_f32() argument
167 (a->numRows != a->numCols) || in arm_mat_solve_lower_triangular_f32()
168 (lt->numRows != a->numRows) ) in arm_mat_solve_lower_triangular_f32()
192 float32_t *pA = a->pData; in arm_mat_solve_lower_triangular_f32()
257 const arm_matrix_instance_f32 * a, in arm_mat_solve_lower_triangular_f32() argument
266 (a->numRows != a->numCols) || in arm_mat_solve_lower_triangular_f32()
[all …]
|
| D | arm_mat_solve_upper_triangular_f32.c | 56 const arm_matrix_instance_f32 * a, in arm_mat_solve_upper_triangular_f32() argument
66 (a->numRows != a->numCols) || in arm_mat_solve_upper_triangular_f32()
67 (ut->numRows != a->numRows) ) in arm_mat_solve_upper_triangular_f32()
84 float32_t *pA = a->pData; in arm_mat_solve_upper_triangular_f32()
153 const arm_matrix_instance_f32 * a, in arm_mat_solve_upper_triangular_f32() argument
163 (a->numRows != a->numCols) || in arm_mat_solve_upper_triangular_f32()
164 (ut->numRows != a->numRows) ) in arm_mat_solve_upper_triangular_f32()
181 float32_t *pA = a->pData; in arm_mat_solve_upper_triangular_f32()
249 const arm_matrix_instance_f32 * a, in arm_mat_solve_upper_triangular_f32() argument
259 (a->numRows != a->numCols) || in arm_mat_solve_upper_triangular_f32()
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/drivers/casper/ |
| D | fsl_casper.c | 170 #define add(c1, c0, a, b) \ argument
175 _t = a + b; \
176 c1 = (uint32_t)(_t < a); \
181 #define add_cout(carry, c, a, b) add((carry), (c), (a), (b)) argument
183 #define add_cout_cin(carryout, c, a, b, carryin) \ argument
186 uint64_t _t = (uint64_t)(a) + (b) + (carryin); \
191 #define sub_borrowout(borrow, c, a, b) \ argument
194 uint32_t _b = (uint32_t)((b) > (a)); \
195 (c) = (a) - (b); \
199 #define sub_borrowin_borrowout(borrowout, c, a, b, borrowin) \ argument
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/components/power_manager/ |
| D | README.md | 14 ## 1. Introduction <a id="introduction"></a>
16 …CU low-power state, peripheral, memory or clock. Each of these states can be specific to a device.
18 …a software framework available for bare-metal code and FreeRTOS applications, aiming at facilitati…
22 ## 2. Glossary <a id="glossary"></a>
32 ## 3. SDK Power Manager <a id="sdkpm"></a>
34 ### 1. Features <a id="features"></a>
44 …tch the constraints of the low-power state, the SDK Power Manager will find a lighter low-power st…
50 ### 2. Architecture <a id="architecture"></a>
60 …stead, the application defines the resource constraints to keep enabled for a given low-power stat…
72 - **PM_RegisterNotify** --> OPTIONAL ; Registers a notify element into the selected group. The call…
[all …]
|
| /hal_nxp-latest/mcux/mcux-sdk/utilities/debug_console_lite/ |
| D | fsl_debug_console.c | 51 typedef int (*PUTCHAR_FUNC)(int a);
304 long long int a; in DbgConsole_ConvertRadixNumToString() local
313 int a; in DbgConsole_ConvertRadixNumToString()
335 a = 0; in DbgConsole_ConvertRadixNumToString()
343 a = 0; in DbgConsole_ConvertRadixNumToString()
352 (void)a; in DbgConsole_ConvertRadixNumToString()
368 a = *(long long int *)nump; in DbgConsole_ConvertRadixNumToString()
370 a = *(int *)nump; in DbgConsole_ConvertRadixNumToString()
372 if (a == 0) in DbgConsole_ConvertRadixNumToString()
378 while (a != 0) in DbgConsole_ConvertRadixNumToString()
[all …]
|
