/third_party/mesa3d/src/gallium/drivers/swr/rasterizer/core/ |
D | api.cpp | 344 pCurDrawContext->pState = &pContext->dsRing[dsIndex]; in GetDrawContext() 356 CopyState(*pCurDrawContext->pState, *pPrevDrawContext->pState); in GetDrawContext() 359 SWR_ASSERT(pCurDrawContext->pState->pArena->IsEmpty() == true); in GetDrawContext() 361 pCurDrawContext->pState->pPrivateState = nullptr; in GetDrawContext() 369 pCurDrawContext->pState = pPrevDrawContext->pState; in GetDrawContext() 375 SWR_ASSERT(pCurDrawContext->pState->pArena->IsEmpty() == true); in GetDrawContext() 412 SWR_ASSERT(pDC->pState != nullptr); in GetDrawState() 414 return &pDC->pState->state; in GetDrawState() 497 API_STATE* pState = GetDrawState(pContext); in SetupDefaultState() local 499 pState->rastState.cullMode = SWR_CULLMODE_NONE; in SetupDefaultState() [all …]
|
/third_party/mesa3d/src/gallium/drivers/swr/rasterizer/memory/ |
D | TilingFunctions.h | 391 const SWR_SURFACE_STATE *pState, 394 const SWR_FORMAT_INFO &info = GetFormatInfo(pState->format); 399 lodOffset = pState->lodOffsets[0][lod]; 403 ComputeLODOffset1D(info, pState->width, pState->halign, lod, lodOffset); 406 xOffsetBytes = (array * pState->qpitch + lodOffset + x) * info.Bpp; 414 INLINE void AdjustCoordsForMSAA(const SWR_SURFACE_STATE *pState, uint32_t& x, uint32_t& y, uint32_t… 417 if((pState->tileMode == SWR_TILE_MODE_YMAJOR || 418 pState->tileMode == SWR_TILE_MODE_WMAJOR) && 419 pState->bInterleavedSamples) 422 switch(pState->numSamples) [all …]
|
/third_party/cmsis/CMSIS/DSP/Source/FilteringFunctions/ |
D | arm_fir_decimate_f32.c | 137 float32_t *pState = S->pState; /* State pointer */ in arm_fir_decimate_f32() local 153 pStateCurnt = S->pState + (numTaps - 1U); in arm_fir_decimate_f32() 186 px0 = pState; in arm_fir_decimate_f32() 187 px1 = pState + S->M; in arm_fir_decimate_f32() 188 px2 = pState + 2 * S->M; in arm_fir_decimate_f32() 189 px3 = pState + 3 * S->M; in arm_fir_decimate_f32() 272 pState = pState + 4 * S->M; in arm_fir_decimate_f32() 303 px = pState; in arm_fir_decimate_f32() 342 pState = pState + S->M; in arm_fir_decimate_f32() 359 pStateCurnt = S->pState; in arm_fir_decimate_f32() [all …]
|
D | arm_lms_norm_f32.c | 168 float32_t *pState = S->pState; /* State pointer */ in arm_lms_norm_f32() local 192 pStateCurnt = &(S->pState[(numTaps - 1U)]); in arm_lms_norm_f32() 203 px = pState; in arm_lms_norm_f32() 263 px = pState; in arm_lms_norm_f32() 301 x0 = *pState; in arm_lms_norm_f32() 304 pState = pState + 1; in arm_lms_norm_f32() 318 pStateCurnt = S->pState; in arm_lms_norm_f32() 326 tempV = vld1q_f32(pState); in arm_lms_norm_f32() 328 pState += 4; in arm_lms_norm_f32() 341 *pStateCurnt++ = *pState++; in arm_lms_norm_f32() [all …]
|
D | arm_fir_decimate_q15.c | 70 q15_t *pState = S->pState; /* State pointer */ in arm_fir_decimate_q15() local 86 pStateCurnt = S->pState + (numTaps - 1U); in arm_fir_decimate_q15() 133 px0 = pState; in arm_fir_decimate_q15() 134 px1 = pState + S->M; in arm_fir_decimate_q15() 135 px2 = pState + 2 * S->M; in arm_fir_decimate_q15() 136 px3 = pState + 3 * S->M; in arm_fir_decimate_q15() 223 pState = pState + 4 * S->M; in arm_fir_decimate_q15() 248 px = pState; in arm_fir_decimate_q15() 283 pState = pState + S->M; in arm_fir_decimate_q15() 300 pStateCurnt = S->pState; in arm_fir_decimate_q15() [all …]
|
D | arm_fir_decimate_fast_q15.c | 68 q15_t *pState = S->pState; /* State pointer */ in arm_fir_decimate_fast_q15() local 87 pStateCur = S->pState + (numTaps - 1U); in arm_fir_decimate_fast_q15() 109 px0 = pState; in arm_fir_decimate_fast_q15() 110 px1 = pState + S->M; in arm_fir_decimate_fast_q15() 177 pState = pState + S->M * 2; in arm_fir_decimate_fast_q15() 203 px = pState; in arm_fir_decimate_fast_q15() 264 pState = pState + S->M; in arm_fir_decimate_fast_q15() 279 pStateCur = S->pState; in arm_fir_decimate_fast_q15() 286 write_q15x2_ia (&pStateCur, read_q15x2_ia (&pState)); in arm_fir_decimate_fast_q15() 287 write_q15x2_ia (&pStateCur, read_q15x2_ia (&pState)); in arm_fir_decimate_fast_q15() [all …]
|
D | arm_biquad_cascade_df1_q15.c | 73 q15_t *pState = S->pState; /* pState pointer initialization */ in arm_biquad_cascade_df1_q15() local 115 inVec0[0] = pState[1]; in arm_biquad_cascade_df1_q15() 116 inVec0[1] = pState[0]; in arm_biquad_cascade_df1_q15() 117 inVec0[6] = pState[3]; in arm_biquad_cascade_df1_q15() 118 inVec0[7] = pState[2]; in arm_biquad_cascade_df1_q15() 246 pState[0] = vgetq_lane_s16(inVec0, 4); in arm_biquad_cascade_df1_q15() 247 pState[1] = vgetq_lane_s16(inVec0, 3); in arm_biquad_cascade_df1_q15() 248 pState[3] = out; in arm_biquad_cascade_df1_q15() 249 pState[2] = out1; in arm_biquad_cascade_df1_q15() 268 pState[0] = vgetq_lane_s16(inVec0, 3); in arm_biquad_cascade_df1_q15() [all …]
|
D | arm_iir_lattice_q31.c | 62 q31_t *pState = S->pState; /* State pointer */ in arm_iir_lattice_q31() local 90 px1 = pState; in arm_iir_lattice_q31() 93 px2 = pState; in arm_iir_lattice_q31() 220 pState = pState + 1U; in arm_iir_lattice_q31() 230 pStateCur = &S->pState[0]; in arm_iir_lattice_q31() 231 pState = &S->pState[blockSize]; in arm_iir_lattice_q31() 241 *pStateCur++ = *pState++; in arm_iir_lattice_q31() 242 *pStateCur++ = *pState++; in arm_iir_lattice_q31() 243 *pStateCur++ = *pState++; in arm_iir_lattice_q31() 244 *pStateCur++ = *pState++; in arm_iir_lattice_q31() [all …]
|
D | arm_lms_f32.c | 174 float32_t *pState = S->pState; /* State pointer */ in arm_lms_f32() local 192 pStateCurnt = &(S->pState[(numTaps - 1U)]); in arm_lms_f32() 202 px = pState; in arm_lms_f32() 255 px = pState; in arm_lms_f32() 294 pState = pState + 1; in arm_lms_f32() 306 pStateCurnt = S->pState; in arm_lms_f32() 314 tempV = vld1q_f32(pState); in arm_lms_f32() 316 pState += 4; in arm_lms_f32() 329 *pStateCurnt++ = *pState++; in arm_lms_f32() 346 float32_t *pState = S->pState; /* State pointer */ in arm_lms_f32() local [all …]
|
D | arm_biquad_cascade_df1_q31.c | 73 q31_t *pState = S->pState; /* pState pointer initialization */ in arm_biquad_cascade_df1_q31() local 115 inVec0[0] = pState[1]; in arm_biquad_cascade_df1_q31() 116 inVec0[1] = pState[0]; in arm_biquad_cascade_df1_q31() 118 stateVec[2] = pState[3]; in arm_biquad_cascade_df1_q31() 119 stateVec[3] = pState[2]; in arm_biquad_cascade_df1_q31() 222 pState[0] = inVec0[1]; in arm_biquad_cascade_df1_q31() 223 pState[1] = inVec0[0]; in arm_biquad_cascade_df1_q31() 224 pState[3] = out; in arm_biquad_cascade_df1_q31() 225 pState[2] = out1; in arm_biquad_cascade_df1_q31() 259 pState[0] = inVec0[2]; in arm_biquad_cascade_df1_q31() [all …]
|
D | arm_fir_decimate_q31.c | 69 q31_t *pState = S->pState; /* State pointer */ in arm_fir_decimate_q31() local 85 pStateCurnt = S->pState + (numTaps - 1U); in arm_fir_decimate_q31() 117 px0 = pState; in arm_fir_decimate_q31() 118 px1 = pState + S->M; in arm_fir_decimate_q31() 119 px2 = pState + 2 * S->M; in arm_fir_decimate_q31() 120 px3 = pState + 3 * S->M; in arm_fir_decimate_q31() 209 pState = pState + 4 * S->M; in arm_fir_decimate_q31() 234 px = pState; in arm_fir_decimate_q31() 273 pState = pState + S->M; in arm_fir_decimate_q31() 289 pStateCurnt = S->pState; in arm_fir_decimate_q31() [all …]
|
D | arm_fir_interpolate_f32.c | 142 float32_t *pState = S->pState; /* State pointer */ in arm_fir_interpolate2_f32_mve() local 158 pStateCurnt = S->pState + (phaseLen - 1U); in arm_fir_interpolate2_f32_mve() 175 ptr1 = pState; in arm_fir_interpolate2_f32_mve() 226 pState = pState + 1; in arm_fir_interpolate2_f32_mve() 242 pStateCurnt = S->pState; in arm_fir_interpolate2_f32_mve() 246 vst1q(pStateCurnt, vldrwq_f32(pState)); in arm_fir_interpolate2_f32_mve() 247 pState += 4; in arm_fir_interpolate2_f32_mve() 255 vstrwq_p_f32(pStateCurnt, vldrwq_f32(pState), p0); in arm_fir_interpolate2_f32_mve() 265 float32_t *pState = S->pState; /* State pointer */ in arm_fir_interpolate_f32() local 290 pStateCurnt = S->pState + (phaseLen - 1U); in arm_fir_interpolate_f32() [all …]
|
D | arm_iir_lattice_q15.c | 63 q15_t *pState = S->pState; /* State pointer */ in arm_iir_lattice_q15() local 96 px1 = pState; in arm_iir_lattice_q15() 99 px2 = pState; in arm_iir_lattice_q15() 259 pState = pState + 1U; in arm_iir_lattice_q15() 269 pStateCur = &S->pState[0]; in arm_iir_lattice_q15() 270 pState = &S->pState[blockSize]; in arm_iir_lattice_q15() 280 write_q15x2_ia (&pStateCur, read_q15x2_ia (&pState)); in arm_iir_lattice_q15() 281 write_q15x2_ia (&pStateCur, read_q15x2_ia (&pState)); in arm_iir_lattice_q15() 299 *pStateCur++ = *pState++; in arm_iir_lattice_q15() 321 px1 = pState; in arm_iir_lattice_q15() [all …]
|
D | arm_iir_lattice_f32.c | 127 float32_t *pState = S->pState; /* State pointer */ in arm_iir_lattice_f32() local 158 px1 = pState; in arm_iir_lattice_f32() 161 px2 = pState; in arm_iir_lattice_f32() 302 pState = pState + 1U; in arm_iir_lattice_f32() 312 pStateCur = &S->pState[0]; in arm_iir_lattice_f32() 313 pState = &S->pState[blockSize]; in arm_iir_lattice_f32() 323 *pStateCur++ = *pState++; in arm_iir_lattice_f32() 324 *pStateCur++ = *pState++; in arm_iir_lattice_f32() 325 *pStateCur++ = *pState++; in arm_iir_lattice_f32() 326 *pStateCur++ = *pState++; in arm_iir_lattice_f32() [all …]
|
D | arm_fir_fast_q31.c | 68 q31_t *pState = S->pState; /* State pointer */ in arm_fir_fast_q31() local 84 pStateCurnt = &(S->pState[(numTaps - 1U)]); in arm_fir_fast_q31() 113 px = pState; in arm_fir_fast_q31() 227 pState = pState + 4U; in arm_fir_fast_q31() 252 px = pState; in arm_fir_fast_q31() 271 pState = pState + 1U; in arm_fir_fast_q31() 282 pStateCurnt = S->pState; in arm_fir_fast_q31() 292 *pStateCurnt++ = *pState++; in arm_fir_fast_q31() 293 *pStateCurnt++ = *pState++; in arm_fir_fast_q31() 294 *pStateCurnt++ = *pState++; in arm_fir_fast_q31() [all …]
|
D | arm_biquad_cascade_df1_f32.c | 175 float32_t *pState = S->pState; /* pState pointer */ in arm_biquad_cascade_df1_f32() local 189 Xn1 = pState[0]; in arm_biquad_cascade_df1_f32() 190 Xn2 = pState[1]; in arm_biquad_cascade_df1_f32() 191 Yn1 = pState[2]; in arm_biquad_cascade_df1_f32() 192 Yn2 = pState[3]; in arm_biquad_cascade_df1_f32() 320 *pState++ = Xn1; in arm_biquad_cascade_df1_f32() 321 *pState++ = Xn2; in arm_biquad_cascade_df1_f32() 322 *pState++ = Yn1; in arm_biquad_cascade_df1_f32() 323 *pState++ = Yn2; in arm_biquad_cascade_df1_f32() 353 float32_t *pState = S->pState; /* pState pointer */ in arm_biquad_cascade_df1_f32() local [all …]
|
D | arm_fir_fast_q15.c | 66 q15_t *pState = S->pState; /* State pointer */ in arm_fir_fast_q15() local 82 pStateCurnt = &(S->pState[(numTaps - 1U)]); in arm_fir_fast_q15() 111 px = pState; in arm_fir_fast_q15() 235 pState = pState + 4U; in arm_fir_fast_q15() 260 px = pState; in arm_fir_fast_q15() 279 pState = pState + 1U; in arm_fir_fast_q15() 290 pStateCurnt = S->pState; in arm_fir_fast_q15() 300 *pStateCurnt++ = *pState++; in arm_fir_fast_q15() 301 *pStateCurnt++ = *pState++; in arm_fir_fast_q15() 302 *pStateCurnt++ = *pState++; in arm_fir_fast_q15() [all …]
|
D | arm_fir_interpolate_q31.c | 66 q31_t *pState = S->pState; /* State pointer */ in arm_fir_interpolate_q31() local 84 pStateCurnt = S->pState + ((q31_t) phaseLen - 1); in arm_fir_interpolate_q31() 107 ptr1 = pState; in arm_fir_interpolate_q31() 316 pState = pState + 1; in arm_fir_interpolate_q31() 332 pStateCurnt = S->pState; in arm_fir_interpolate_q31() 336 vst1q(pStateCurnt, vldrwq_s32(pState)); in arm_fir_interpolate_q31() 337 pState += 4; in arm_fir_interpolate_q31() 345 vstrwq_p_s32(pStateCurnt, vldrwq_s32(pState), p0); in arm_fir_interpolate_q31() 358 q31_t *pState = S->pState; /* State pointer */ in arm_fir_interpolate_q31() local 376 pStateCur = S->pState + (phaseLen - 1U); in arm_fir_interpolate_q31() [all …]
|
D | arm_fir_decimate_fast_q31.c | 68 q31_t *pState = S->pState; /* State pointer */ in arm_fir_decimate_fast_q31() local 86 pStateCur = S->pState + (numTaps - 1U); in arm_fir_decimate_fast_q31() 112 px0 = pState; in arm_fir_decimate_fast_q31() 113 px1 = pState + S->M; in arm_fir_decimate_fast_q31() 114 px2 = pState + 2 * S->M; in arm_fir_decimate_fast_q31() 115 px3 = pState + 3 * S->M; in arm_fir_decimate_fast_q31() 218 pState = pState + S->M * 4; in arm_fir_decimate_fast_q31() 255 px0 = pState; in arm_fir_decimate_fast_q31() 334 pState = pState + S->M; in arm_fir_decimate_fast_q31() 348 pStateCur = S->pState; in arm_fir_decimate_fast_q31() [all …]
|
D | arm_biquad_cascade_df1_32x64_q31.c | 186 q63_t *pState = S->pState; /* state pointer initialization */ in arm_biquad_cas_df1_32x64_q31_scalar() local 209 Xn1 = (q31_t) (pState[0]); in arm_biquad_cas_df1_32x64_q31_scalar() 210 Xn2 = (q31_t) (pState[1]); in arm_biquad_cas_df1_32x64_q31_scalar() 211 Yn1 = pState[2]; in arm_biquad_cas_df1_32x64_q31_scalar() 212 Yn2 = pState[3]; in arm_biquad_cas_df1_32x64_q31_scalar() 275 *pState++ = (q63_t) Xn1; in arm_biquad_cas_df1_32x64_q31_scalar() 276 *pState++ = (q63_t) Xn2; in arm_biquad_cas_df1_32x64_q31_scalar() 277 *pState++ = Yn1; in arm_biquad_cas_df1_32x64_q31_scalar() 278 *pState++ = Yn2; in arm_biquad_cas_df1_32x64_q31_scalar() 292 q63_t *pState = S->pState; /* state pointer initialization */ in arm_biquad_cas_df1_32x64_q31() local [all …]
|
D | arm_lms_norm_q31.c | 73 q31_t *pState = S->pState; /* State pointer */ in arm_lms_norm_q31() local 97 pStateCurnt = &(S->pState[(numTaps - 1U)]); in arm_lms_norm_q31() 108 px = pState; in arm_lms_norm_q31() 192 px = pState; in arm_lms_norm_q31() 252 x0 = *pState; in arm_lms_norm_q31() 255 pState = pState + 1; in arm_lms_norm_q31() 270 pStateCurnt = S->pState; in arm_lms_norm_q31() 280 *pStateCurnt++ = *pState++; in arm_lms_norm_q31() 281 *pStateCurnt++ = *pState++; in arm_lms_norm_q31() 282 *pStateCurnt++ = *pState++; in arm_lms_norm_q31() [all …]
|
/third_party/cmsis/CMSIS/DSP/Source/TransformFunctions/ |
D | arm_dct4_q31.c | 56 q31_t * pState, in arm_dct4_q31() argument 97 pS1 = pState; in arm_dct4_q31() 100 pS2 = pState + (S->N - 1U); in arm_dct4_q31() 138 pS1 = pState; in arm_dct4_q31() 162 arm_rfft_q31 (S->pRfft, pInlineBuffer, pState); in arm_dct4_q31() 167 arm_cmplx_mult_cmplx_q31 (pState, weights, pState, S->N); in arm_dct4_q31() 171 arm_shift_q31 (pState, 2, pState, S->N * 2); in arm_dct4_q31() 186 pS1 = pState; in arm_dct4_q31() 292 pS1 = pState; in arm_dct4_q31() 311 arm_rfft_q31 (S->pRfft, pInlineBuffer, pState); in arm_dct4_q31() [all …]
|
D | arm_dct4_q15.c | 53 q15_t * pState, in arm_dct4_q15() argument 94 pS1 = pState; in arm_dct4_q15() 97 pS2 = pState + (S->N - 1U); in arm_dct4_q15() 135 pS1 = pState; in arm_dct4_q15() 159 arm_rfft_q15 (S->pRfft, pInlineBuffer, pState); in arm_dct4_q15() 164 arm_cmplx_mult_cmplx_q15 (pState, weights, pState, S->N); in arm_dct4_q15() 168 arm_shift_q15 (pState, 2, pState, S->N * 2); in arm_dct4_q15() 183 pS1 = pState; in arm_dct4_q15() 289 pS1 = pState; in arm_dct4_q15() 308 arm_rfft_q15 (S->pRfft, pInlineBuffer, pState); in arm_dct4_q15() [all …]
|
D | arm_dct4_f32.c | 129 float32_t * pState, in arm_dct4_f32() argument 170 pS1 = pState; in arm_dct4_f32() 173 pS2 = pState + (S->N - 1U); in arm_dct4_f32() 211 pS1 = pState; in arm_dct4_f32() 235 arm_rfft_f32 (S->pRfft, pInlineBuffer, pState); in arm_dct4_f32() 240 arm_cmplx_mult_cmplx_f32 (pState, weights, pState, S->N); in arm_dct4_f32() 255 pS1 = pState; in arm_dct4_f32() 361 pS1 = pState; in arm_dct4_f32() 380 arm_rfft_f32 (S->pRfft, pInlineBuffer, pState); in arm_dct4_f32() 385 arm_cmplx_mult_cmplx_f32 (pState, weights, pState, S->N); in arm_dct4_f32() [all …]
|
/third_party/cmsis/CMSIS/DSP/Include/dsp/ |
D | filtering_functions.h | 59 …q7_t *pState; /**< points to the state variable array. The array is of length numTaps+b… member 69 …q15_t *pState; /**< points to the state variable array. The array is of length numTaps+… member 79 …q31_t *pState; /**< points to the state variable array. The array is of length numTaps+… member 89 …float32_t *pState; /**< points to the state variable array. The array is of length numTaps+bloc… member 121 q7_t * pState, 169 q15_t * pState, 213 q31_t * pState, 241 float32_t * pState, 250 …q15_t *pState; /**< Points to the array of state coefficients. The array is of length 4… member 261 …q31_t *pState; /**< Points to the array of state coefficients. The array is of length 4… member [all …]
|