Home
last modified time | relevance | path

Searched refs:simdscalar (Results 1 – 21 of 21) sorted by relevance

/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
Ddepthstencil.h33 void StencilOp(SWR_STENCILOP op, simdscalar const &mask, simdscalar const &stencilRefps, simdscalar… in StencilOp()
73 …simdscalar stencilinvert = _simd_andnot_ps(stencilps, _simd_cmpeq_ps(_simd_setzero_ps(), _simd_set… in StencilOp()
84 simdscalar QuantizeDepth(simdscalar const &depth) in QuantizeDepth()
102 simdscalar result = _simd_mul_ps(depth, _simd_set1_ps(quantize)); in QuantizeDepth()
119 simdscalar DepthStencilTest(const API_STATE* pState, in DepthStencilTest()
120 …bool frontFacing, uint32_t viewportIndex, simdscalar const &iZ, uint8_t* pDepthBase, simdscalar co… in DepthStencilTest()
121 uint8_t *pStencilBase, simdscalar* pStencilMask) in DepthStencilTest()
129 simdscalar depthResult = _simd_set1_ps(-1.0f); in DepthStencilTest()
130 simdscalar zbuf; in DepthStencilTest()
133 simdscalar vMinZ = _simd_broadcast_ss(&pViewport->minZ); in DepthStencilTest()
[all …]
Dformat_types.h40 static simdscalar loadSOA(const uint8_t *pSrc) = delete;
41 static void storeSOA(uint8_t *pDst, simdscalar const &src) = delete;
42 static simdscalar unpack(simdscalar &in) = delete;
43 static simdscalar pack(simdscalar &in) = delete;
60 static simdscalar loadSOA(const uint8_t *pSrc) { return _simd_setzero_ps(); }
61 static void storeSOA(uint8_t *pDst, simdscalar const &src) { return; }
62 static simdscalar unpack(simdscalar &in) { return _simd_setzero_ps(); }
63 static simdscalar pack(simdscalar &in) { return _simd_setzero_ps(); }
80 static simdscalar loadSOA(const uint8_t *pSrc)
91 static void storeSOA(uint8_t *pDst, simdscalar const &src)
[all …]
Dformat_utils.h85 …d vTranspose3x8(simd4scalar (&vDst)[8], const simdscalar &vSrc0, const simdscalar &vSrc1, const si… in vTranspose3x8()
87 simdscalar r0r2 = _simd_unpacklo_ps(vSrc0, vSrc2); //x0z0x1z1 x4z4x5z5 in vTranspose3x8()
88 simdscalar r1rx = _simd_unpacklo_ps(vSrc1, _simd_setzero_ps()); //y0w0y1w1 y4w4y5w5 in vTranspose3x8()
89 simdscalar r02r1xlolo = _simd_unpacklo_ps(r0r2, r1rx); //x0y0z0w0 x4y4z4w4 in vTranspose3x8()
90 simdscalar r02r1xlohi = _simd_unpackhi_ps(r0r2, r1rx); //x1y1z1w1 x5y5z5w5 in vTranspose3x8()
94 simdscalar r02r1xhilo = _simd_unpacklo_ps(r0r2, r1rx); //x2y2z2w2 x6y6z6w6 in vTranspose3x8()
95 simdscalar r02r1xhihi = _simd_unpackhi_ps(r0r2, r1rx); //x3y3z3w3 x7y7z7w7 in vTranspose3x8()
109 …4x8(simd4scalar (&vDst)[8], const simdscalar &vSrc0, const simdscalar &vSrc1, const simdscalar &vS… in vTranspose4x8()
111 simdscalar r0r2 = _simd_unpacklo_ps(vSrc0, vSrc2); //x0z0x1z1 x4z4x5z5 in vTranspose4x8()
112 simdscalar r1rx = _simd_unpacklo_ps(vSrc1, vSrc3); //y0w0y1w1 y4w4y5w5 in vTranspose4x8()
[all …]
Dcontext.h324 simdscalar vIa;
325 simdscalar vIb;
326 simdscalar vIc;
328 simdscalar vJa;
329 simdscalar vJb;
330 simdscalar vJc;
332 simdscalar vZa;
333 simdscalar vZb;
334 simdscalar vZc;
336 simdscalar vRecipDet;
[all …]
Dbackend_impl.h53 …mputeUserClipMask(uint8_t clipMask, float* pUserClipBuffer, simdscalar const &vI, simdscalar const… in ComputeUserClipMask()
55 simdscalar vClipMask = _simd_setzero_ps(); in ComputeUserClipMask()
61 simdscalar vA = _simd_broadcast_ss(pUserClipBuffer++); in ComputeUserClipMask()
62 simdscalar vB = _simd_broadcast_ss(pUserClipBuffer++); in ComputeUserClipMask()
63 simdscalar vC = _simd_broadcast_ss(pUserClipBuffer++); in ComputeUserClipMask()
66 simdscalar vInterp = vplaneps(vA, vB, vC, vI, vJ); in ComputeUserClipMask()
69 simdscalar vCull = _simd_cmp_ps(_simd_setzero_ps(), vInterp, _CMP_NLE_UQ); in ComputeUserClipMask()
238 …simdscalar shufRes = _mm256_shuffle_ps(_mm256_castsi256_ps(hiToLow), _mm256_castsi256_ps(hiToLow),… in generateInputCoverage()
292 …INLINE generateInputCoverage(const uint64_t *const coverageMask, simdscalar &inputCoverage, const … in generateInputCoverage()
304 …INLINE generateInputCoverage(const uint64_t *const coverageMask, simdscalar &inputCoverage, const …
[all …]
Dformat_conversion.h44 simdscalar vComp = _simd_load_ps((const float*)(pSrc + comp*sizeof(simdscalar))); in LoadSOA()
56 simdscalar vComp = FormatTraits<SrcFormat>::loadSOA(comp, pSrc); in LoadSOA()
82 INLINE simdscalar Clamp(simdscalar const &vC, uint32_t Component) in Clamp()
84 simdscalar vComp = vC; in Clamp()
129 INLINE simdscalar Normalize(simdscalar const &vC, uint32_t Component) in Normalize()
131 simdscalar vComp = vC; in Normalize()
153 simdscalar vComp = src.v[FormatTraits<DstFormat>::swizzle(comp)]; in StoreSOA()
164 _simd_store_ps((float*)(pDst + comp*sizeof(simdscalar)), vComp); in StoreSOA()
171 simdscalar vComp = src.v[FormatTraits<DstFormat>::swizzle(comp)]; in StoreSOA()
Dstate.h297 simdscalar* pDomainU; // IN: (SIMD) Domain Point U coords
298 simdscalar* pDomainV; // IN: (SIMD) Domain Point V coords
300 …simdscalar* pOutputData; // OUT: (SIMD) Vertex Attributes (2D array of vectors, one row per…
319 simdscalar UL;
320 simdscalar center;
321 simdscalar sample;
322 simdscalar centroid;
335 simdscalar vZ; // INOUT: z location of pixels
337 simdscalar inputMask; // IN: input coverage mask for all samples
893 simdvector& vSrc, simdvector& vSrc1, simdscalar& vSrc0Alpha, uint32_t sample,
[all …]
Dpa_avx.cpp37 INLINE simd4scalar swizzleLane0(const simdscalar &x, const simdscalar &y, const simdscalar &z, cons… in swizzleLane0()
39 simdscalar tmp0 = _mm256_unpacklo_ps(x, z); in swizzleLane0()
40 simdscalar tmp1 = _mm256_unpacklo_ps(y, w); in swizzleLane0()
44 INLINE simd4scalar swizzleLane1(const simdscalar &x, const simdscalar &y, const simdscalar &z, cons… in swizzleLane1()
46 simdscalar tmp0 = _mm256_unpacklo_ps(x, z); in swizzleLane1()
47 simdscalar tmp1 = _mm256_unpacklo_ps(y, w); in swizzleLane1()
51 INLINE simd4scalar swizzleLane2(const simdscalar &x, const simdscalar &y, const simdscalar &z, cons… in swizzleLane2()
53 simdscalar tmp0 = _mm256_unpackhi_ps(x, z); in swizzleLane2()
54 simdscalar tmp1 = _mm256_unpackhi_ps(y, w); in swizzleLane2()
58 INLINE simd4scalar swizzleLane3(const simdscalar &x, const simdscalar &y, const simdscalar &z, cons… in swizzleLane3()
[all …]
Dfrontend.h240 simdscalar m00 = _simd_load1_ps(&vpMatrices.m00[0]); in viewportTransform()
241 simdscalar m30 = _simd_load1_ps(&vpMatrices.m30[0]); in viewportTransform()
242 simdscalar m11 = _simd_load1_ps(&vpMatrices.m11[0]); in viewportTransform()
243 simdscalar m31 = _simd_load1_ps(&vpMatrices.m31[0]); in viewportTransform()
244 simdscalar m22 = _simd_load1_ps(&vpMatrices.m22[0]); in viewportTransform()
245 simdscalar m32 = _simd_load1_ps(&vpMatrices.m32[0]); in viewportTransform()
281 simdscalar m00 = _simd_i32gather_ps(&vpMatrices.m00[0], vViewportIdx, 4); in viewportTransform()
282 simdscalar m30 = _simd_i32gather_ps(&vpMatrices.m30[0], vViewportIdx, 4); in viewportTransform()
283 simdscalar m11 = _simd_i32gather_ps(&vpMatrices.m11[0], vViewportIdx, 4); in viewportTransform()
284 simdscalar m31 = _simd_i32gather_ps(&vpMatrices.m31[0], vViewportIdx, 4); in viewportTransform()
[all …]
Dbackend.cpp221 simdscalar vYSamplePosUL = _simd_add_ps(vULOffsetsY, _simd_set1_ps(static_cast<float>(y))); in BackendNullPS()
223 const simdscalar dy = _simd_set1_ps(static_cast<float>(SIMD_TILE_Y_DIM)); in BackendNullPS()
227 simdscalar vXSamplePosUL = _simd_add_ps(vULOffsetsX, _simd_set1_ps(static_cast<float>(x))); in BackendNullPS()
229 const simdscalar dx = _simd_set1_ps(static_cast<float>(SIMD_TILE_X_DIM)); in BackendNullPS()
252 … const simdscalar z = _simd_load_ps(reinterpret_cast<const float *>(pDepthSample)); in BackendNullPS()
280 simdscalar vCoverageMask = _simd_vmask_ps(coverageMask); in BackendNullPS()
281 simdscalar stencilPassMask = vCoverageMask; in BackendNullPS()
284 …simdscalar depthPassMask = DepthStencilTest(&state, work.triFlags.frontFacing, work.triFlags.viewp… in BackendNullPS()
Dbackend_singlesample.cpp65 const simdscalar dy = _simd_set1_ps(static_cast<float>(SIMD_TILE_Y_DIM)); in BackendSingleSample()
72 const simdscalar dx = _simd_set1_ps(static_cast<float>(SIMD_TILE_X_DIM)); in BackendSingleSample()
87 … const simdscalar z = _simd_load_ps(reinterpret_cast<const float *>(pDepthBuffer)); in BackendSingleSample()
120 simdscalar vCoverageMask = _simd_vmask_ps(coverageMask); in BackendSingleSample()
121 simdscalar depthPassMask = vCoverageMask; in BackendSingleSample()
122 simdscalar stencilPassMask = vCoverageMask; in BackendSingleSample()
Dbackend_sample.cpp65 const simdscalar dy = _simd_set1_ps(static_cast<float>(SIMD_TILE_Y_DIM)); in BackendSampleRate()
72 const simdscalar dx = _simd_set1_ps(static_cast<float>(SIMD_TILE_X_DIM)); in BackendSampleRate()
108 … const simdscalar z = _simd_load_ps(reinterpret_cast<const float *>(pDepthSample)); in BackendSampleRate()
136 simdscalar vCoverageMask = _simd_vmask_ps(coverageMask); in BackendSampleRate()
137 simdscalar depthPassMask = vCoverageMask; in BackendSampleRate()
138 simdscalar stencilPassMask = vCoverageMask; in BackendSampleRate()
Dtilemgr.cpp297 simdscalar valR = _simd_broadcast_ss(&pClearData[0]); in ClearColorHotTile()
298 simdscalar valG = _simd_broadcast_ss(&pClearData[1]); in ClearColorHotTile()
299 simdscalar valB = _simd_broadcast_ss(&pClearData[2]); in ClearColorHotTile()
300 simdscalar valA = _simd_broadcast_ss(&pClearData[3]); in ClearColorHotTile()
328 simdscalar valZ = _simd_broadcast_ss(&pClearData[0]); in ClearDepthHotTile()
Dblend.h82 simdscalar oneMinusSrcA = _simd_sub_ps(_simd_set1_ps(1.0), src.w); in GenerateBlendFactor()
98 simdscalar oneMinusDstA = _simd_sub_ps(_simd_set1_ps(1.0), dst.w); in GenerateBlendFactor()
108 simdscalar sat = _simd_min_ps(src.w, _simd_sub_ps(_simd_set1_ps(1.0), dst.w)); in GenerateBlendFactor()
Dbackend_clear.cpp102 simdscalar vComp; in ClearMacroTile()
Dpa.h63 typedef simdscalar SIMDSCALAR;
711 … simdscalar t = useAlternateOffset ? _simd16_extract_ps(temp, 1) : _simd16_extract_ps(temp, 0); in Assemble()
1312 simdscalar temp = _simd_mask_i32gather_ps( in Assemble()
Dfrontend.cpp1132 simdscalar* pDSOutput;
1290 … gt_pTessellationThreadData->pDSOutput = (simdscalar*)AlignedMalloc(requiredAllocSize, 64); in TessellationStages()
1304 dsContext.pDomainU = (simdscalar*)tsData.pDomainPointsU; in TessellationStages()
1305 dsContext.pDomainV = (simdscalar*)tsData.pDomainPointsV; in TessellationStages()
Dbinner.cpp284 … TransposeVertices(simd4scalar(&dst)[8], const simdscalar &src0, const simdscalar &src1, const sim… in TransposeVertices()
/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/
Dsimdintrin.h193 void _simd_mov(simdscalar &r, unsigned int rlane, simdscalar& s, unsigned int slane) in _simd_mov()
206 void _simdvec_mov(simdvector& r, const simdscalar& s) in _simdvec_mov()
245 SIMDINLINE simdscalar vplaneps(simdscalar const &vA, simdscalar const &vB, simdscalar const &vC, si… in vplaneps()
247 simdscalar vOut = _simd_fmadd_ps(vA, vX, vC); in vplaneps()
267 static SIMDINLINE simdscalar InterpolateComponent(simdscalar const &vI, simdscalar const &vJ, const… in InterpolateComponent()
273 simdscalar vA = _simd_broadcast_ss(pInterpA); in InterpolateComponent()
274 simdscalar vB = _simd_broadcast_ss(pInterpB); in InterpolateComponent()
275 simdscalar vC = _simd_broadcast_ss(pInterpC); in InterpolateComponent()
277 simdscalar vk = _simd_sub_ps(_simd_sub_ps(_simd_set1_ps(1.0f), vI), vJ); in InterpolateComponent()
287 static SIMDINLINE simdscalar InterpolateComponentFlat(const float *pInterpBuffer) in InterpolateComponentFlat()
[all …]
Dintrin.h51 typedef simd8scalar simdscalar; typedef
/external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/
DStoreTile.h696 static const uint32_t offset = sizeof(simdscalar);
699 …simdscalar vComp0 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(0))*offs…
700 …simdscalar vComp1 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(1))*offs…
701 …simdscalar vComp2 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(2))*offs…
702 …simdscalar vComp3 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(3))*offs…
861 static const uint32_t offset = sizeof(simdscalar);
864 …simdscalar vComp0 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(0))*offs…
865 …simdscalar vComp1 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(1))*offs…
866 …simdscalar vComp2 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(2))*offs…