Home
last modified time | relevance | path

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

/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
Ddepthstencil.h34 simdscalar const& mask, in StencilOp()
35 simdscalar const& stencilRefps, in StencilOp()
36 simdscalar& stencilps) in StencilOp()
76 simdscalar stencilinvert = in StencilOp()
87 simdscalar QuantizeDepth(simdscalar const& depth) in QuantizeDepth()
105 simdscalar result = _simd_mul_ps(depth, _simd_set1_ps(quantize)); in QuantizeDepth()
122 simdscalar DepthStencilTest(const API_STATE* pState, in DepthStencilTest()
125 simdscalar const& iZ, in DepthStencilTest()
127 simdscalar const& coverageMask, in DepthStencilTest()
129 simdscalar* pStencilMask) in DepthStencilTest()
[all …]
Dformat_types.h41 static simdscalar loadSOA(const uint8_t* pSrc) = delete;
42 static void storeSOA(uint8_t* pDst, simdscalar const& src) = delete;
43 static simdscalar unpack(simdscalar& in) = delete;
44 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(); }
79 static simdscalar loadSOA(const uint8_t* pSrc)
90 static void storeSOA(uint8_t* pDst, simdscalar const& src)
[all …]
Dformat_utils.h86 const simdscalar& vSrc0, in vTranspose3x8()
87 const simdscalar& vSrc1, in vTranspose3x8()
88 const simdscalar& vSrc2) in vTranspose3x8()
90 simdscalar r0r2 = _simd_unpacklo_ps(vSrc0, vSrc2); // x0z0x1z1 x4z4x5z5 in vTranspose3x8()
91 simdscalar r1rx = _simd_unpacklo_ps(vSrc1, _simd_setzero_ps()); // y0w0y1w1 y4w4y5w5 in vTranspose3x8()
92 simdscalar r02r1xlolo = _simd_unpacklo_ps(r0r2, r1rx); // x0y0z0w0 x4y4z4w4 in vTranspose3x8()
93 simdscalar r02r1xlohi = _simd_unpackhi_ps(r0r2, r1rx); // x1y1z1w1 x5y5z5w5 in vTranspose3x8()
97 simdscalar r02r1xhilo = _simd_unpacklo_ps(r0r2, r1rx); // x2y2z2w2 x6y6z6w6 in vTranspose3x8()
98 simdscalar r02r1xhihi = _simd_unpackhi_ps(r0r2, r1rx); // x3y3z3w3 x7y7z7w7 in vTranspose3x8()
113 const simdscalar& vSrc0, in vTranspose4x8()
[all …]
Dcontext.h351 simdscalar vIa;
352 simdscalar vIb;
353 simdscalar vIc;
355 simdscalar vJa;
356 simdscalar vJb;
357 simdscalar vJc;
359 simdscalar vZa;
360 simdscalar vZb;
361 simdscalar vZc;
363 simdscalar vRecipDet;
[all …]
Dbackend_impl.h62 simdscalar const& vI, in ComputeUserClipMask()
63 simdscalar const& vJ) in ComputeUserClipMask()
65 simdscalar vClipMask = _simd_setzero_ps(); in ComputeUserClipMask()
71 simdscalar vA = _simd_broadcast_ss(pUserClipBuffer++); in ComputeUserClipMask()
72 simdscalar vB = _simd_broadcast_ss(pUserClipBuffer++); in ComputeUserClipMask()
73 simdscalar vC = _simd_broadcast_ss(pUserClipBuffer++); in ComputeUserClipMask()
76 simdscalar vInterp = vplaneps(vA, vB, vC, vI, vJ); in ComputeUserClipMask()
79 simdscalar vCull = _simd_cmp_ps(_simd_setzero_ps(), vInterp, _CMP_NLE_UQ); in ComputeUserClipMask()
319 simdscalar shufRes = _mm256_shuffle_ps( in generateInputCoverage()
381 simdscalar& inputCoverage, in generateInputCoverage()
[all …]
Dpa_avx.cpp37 INLINE simd4scalar swizzleLane0(const simdscalar& x, in swizzleLane0()
38 const simdscalar& y, in swizzleLane0()
39 const simdscalar& z, in swizzleLane0()
40 const simdscalar& w) in swizzleLane0()
42 simdscalar tmp0 = _mm256_unpacklo_ps(x, z); in swizzleLane0()
43 simdscalar tmp1 = _mm256_unpacklo_ps(y, w); in swizzleLane0()
47 INLINE simd4scalar swizzleLane1(const simdscalar& x, in swizzleLane1()
48 const simdscalar& y, in swizzleLane1()
49 const simdscalar& z, in swizzleLane1()
50 const simdscalar& w) in swizzleLane1()
[all …]
Dstate.h328 simdscalar* pDomainU; // IN: (SIMD) Domain Point U coords
329 simdscalar* pDomainV; // IN: (SIMD) Domain Point V coords
331 …simdscalar* pOutputData; // OUT: (SIMD) Vertex Attributes (2D array of vectors, one row per…
352 simdscalar UL;
353 simdscalar center;
354 simdscalar sample;
355 simdscalar centroid;
368 simdscalar vZ; // INOUT: z location of pixels
370 simdscalar inputMask; // IN: input coverage mask for all samples
914 typedef simdscalar(*PFN_QUANTIZE_DEPTH)(simdscalar const &);
[all …]
Dfrontend.h260 simdscalar m00 = _simd_load1_ps(&vpMatrices.m00[0]); in viewportTransform()
261 simdscalar m30 = _simd_load1_ps(&vpMatrices.m30[0]); in viewportTransform()
262 simdscalar m11 = _simd_load1_ps(&vpMatrices.m11[0]); in viewportTransform()
263 simdscalar m31 = _simd_load1_ps(&vpMatrices.m31[0]); in viewportTransform()
264 simdscalar m22 = _simd_load1_ps(&vpMatrices.m22[0]); in viewportTransform()
265 simdscalar m32 = _simd_load1_ps(&vpMatrices.m32[0]); in viewportTransform()
301 simdscalar m00 = _simd_i32gather_ps(&vpMatrices.m00[0], vViewportIdx, 4); in viewportTransform()
302 simdscalar m30 = _simd_i32gather_ps(&vpMatrices.m30[0], vViewportIdx, 4); in viewportTransform()
303 simdscalar m11 = _simd_i32gather_ps(&vpMatrices.m11[0], vViewportIdx, 4); in viewportTransform()
304 simdscalar m31 = _simd_i32gather_ps(&vpMatrices.m31[0], vViewportIdx, 4); in viewportTransform()
[all …]
Dbackend.cpp277 simdscalar vYSamplePosUL = _simd_add_ps(vULOffsetsY, _simd_set1_ps(static_cast<float>(y))); in BackendNullPS()
279 const simdscalar dy = _simd_set1_ps(static_cast<float>(SIMD_TILE_Y_DIM)); in BackendNullPS()
283 simdscalar vXSamplePosUL = _simd_add_ps(vULOffsetsX, _simd_set1_ps(static_cast<float>(x))); in BackendNullPS()
285 const simdscalar dx = _simd_set1_ps(static_cast<float>(SIMD_TILE_X_DIM)); in BackendNullPS()
309 const simdscalar z = in BackendNullPS()
345 simdscalar vCoverageMask = _simd_vmask_ps(coverageMask); in BackendNullPS()
346 simdscalar stencilPassMask = vCoverageMask; in BackendNullPS()
349 simdscalar depthPassMask = DepthStencilTest(&state, in BackendNullPS()
Dbackend_singlesample.cpp77 const simdscalar dy = _simd_set1_ps(static_cast<float>(SIMD_TILE_Y_DIM)); in BackendSingleSample()
84 const simdscalar dx = _simd_set1_ps(static_cast<float>(SIMD_TILE_X_DIM)); in BackendSingleSample()
100 const simdscalar z = in BackendSingleSample()
143 simdscalar vCoverageMask = _simd_vmask_ps(coverageMask); in BackendSingleSample()
144 simdscalar depthPassMask = vCoverageMask; in BackendSingleSample()
145 simdscalar stencilPassMask = vCoverageMask; in BackendSingleSample()
Dbackend_sample.cpp75 const simdscalar dy = _simd_set1_ps(static_cast<float>(SIMD_TILE_Y_DIM)); in BackendSampleRate()
82 const simdscalar dx = _simd_set1_ps(static_cast<float>(SIMD_TILE_X_DIM)); in BackendSampleRate()
124 const simdscalar z = in BackendSampleRate()
160 simdscalar vCoverageMask = _simd_vmask_ps(coverageMask); in BackendSampleRate()
161 simdscalar depthPassMask = vCoverageMask; in BackendSampleRate()
162 simdscalar stencilPassMask = vCoverageMask; in BackendSampleRate()
Dformat_conversion.h148 INLINE simdscalar SIMDCALL Clamp(simdscalar const& v, uint32_t Component) in Clamp()
177 INLINE simdscalar SIMDCALL Normalize(simdscalar const& vComp, uint32_t Component) in Normalize()
Dblend.h87 simdscalar oneMinusSrcA = _simd_sub_ps(_simd_set1_ps(1.0), src.w); in GenerateBlendFactor()
104 simdscalar oneMinusDstA = _simd_sub_ps(_simd_set1_ps(1.0), dst.w); in GenerateBlendFactor()
114 simdscalar sat = _simd_min_ps(src.w, _simd_sub_ps(_simd_set1_ps(1.0), dst.w)); in GenerateBlendFactor()
Dpa.h63 typedef simdscalar SIMDSCALAR;
778 simdscalar t = in Assemble()
1466 simdscalar temp = _simd_mask_i32gather_ps(_simd_setzero_ps(), in Assemble()
Dfrontend.cpp1230 simdscalar* pDSOutput;
1426 (simdscalar*)AlignedMalloc(requiredAllocSize, 64); in TessellationStages()
1440 dsContext.pDomainU = (simdscalar*)tsData.pDomainPointsU; in TessellationStages()
1441 dsContext.pDomainV = (simdscalar*)tsData.pDomainPointsV; in TessellationStages()
Dbinner.cpp287 const simdscalar& src0, in TransposeVertices()
288 const simdscalar& src1, in TransposeVertices()
289 const simdscalar& src2) in TransposeVertices()
/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/
Dsimdintrin.h196 SIMDINLINE simdscalar vplaneps(simdscalar const& vA, in vplaneps()
197 simdscalar const& vB, in vplaneps()
198 simdscalar const& vC, in vplaneps()
199 simdscalar const& vX, in vplaneps()
200 simdscalar const& vY) in vplaneps()
202 simdscalar vOut = _simd_fmadd_ps(vA, vX, vC); in vplaneps()
226 static SIMDINLINE simdscalar InterpolateComponent(simdscalar const& vI, in InterpolateComponent()
227 simdscalar const& vJ, in InterpolateComponent()
241 simdscalar vA = _simd_broadcast_ss(pInterpA); in InterpolateComponent()
242 simdscalar vB = _simd_broadcast_ss(pInterpB); in InterpolateComponent()
[all …]
Dintrin.h54 typedef simd8scalar simdscalar; typedef
/external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/
DStoreTile.h580 static const uint32_t offset = sizeof(simdscalar);
583 …simdscalar vComp0 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(0))*offs…
584 …simdscalar vComp1 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(1))*offs…
585 …simdscalar vComp2 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(2))*offs…
586 …simdscalar vComp3 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(3))*offs…
743 static const uint32_t offset = sizeof(simdscalar);
746 …simdscalar vComp0 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(0))*offs…
747 …simdscalar vComp1 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(1))*offs…
748 …simdscalar vComp2 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(2))*offs…