| /external/mesa3d/src/gallium/drivers/swr/rasterizer/core/ |
| depthstencil.h | 33 void StencilOp(SWR_STENCILOP op, simdscalar mask, simdscalar stencilRefps, simdscalar &stencilps)
73 simdscalar stencilinvert = _simd_andnot_ps(stencilps, _simd_cmpeq_ps(_simd_setzero_ps(), _simd_setzero_ps()));
84 simdscalar QuantizeDepth(simdscalar depth)
102 simdscalar result = _simd_mul_ps(depth, _simd_set1_ps(quantize));
119 simdscalar DepthStencilTest(const API_STATE* pState,
120 bool frontFacing, uint32_t viewportIndex, simdscalar interpZ, uint8_t* pDepthBase, simdscalar coverageMask
[all...] |
| format_types.h | 39 static simdscalar loadSOA(const uint8_t *pSrc) = delete;
40 static void storeSOA(uint8_t *pDst, simdscalar src) = delete;
41 static simdscalar unpack(simdscalar &in) = delete;
42 static simdscalar pack(simdscalar &in) = delete;
59 static simdscalar loadSOA(const uint8_t *pSrc) { return _simd_setzero_ps(); }
60 static void storeSOA(uint8_t *pDst, simdscalar src) { return; }
61 static simdscalar unpack(simdscalar &in) { return _simd_setzero_ps();
[all...] |
| clip.h | 66 void ComputeClipCodes(const API_STATE& state, const simdvector& vertex, simdscalar& clipCodes, simdscalari viewportIndexes)
71 simdscalar vNegW = _simd_mul_ps(vertex.w, _simd_set1_ps(-1.0f));
74 simdscalar vRes = _simd_cmplt_ps(vertex.x, vNegW);
113 simdscalar gbMult = _simd_mul_ps(vNegW, _simd_i32gather_ps(&state.gbState.left[0], viewportIndexes, 4));
151 simdscalar ComputeClipCodeIntersection()
153 simdscalar result = this->clipCodes[0];
161 simdscalar ComputeClipCodeUnion()
163 simdscalar result = this->clipCodes[0];
173 simdscalar clipCodeUnion = ComputeClipCodeUnion();
180 simdscalar clipUnion = ComputeClipCodeUnion()
[all...] |
| context.h | 317 simdscalar vIa;
318 simdscalar vIb;
319 simdscalar vIc;
321 simdscalar vJa;
322 simdscalar vJb;
323 simdscalar vJc;
325 simdscalar vZa;
326 simdscalar vZb;
327 simdscalar vZc;
329 simdscalar vRecipDet
[all...] |
| multisample.h | 66 INLINE static simdscalar vX(uint32_t sampleNum) = delete;
67 INLINE static simdscalar vY(uint32_t sampleNum) = delete;
92 INLINE static simdscalar vX(uint32_t sampleNum)
94 static const simdscalar X = _simd_set1_ps(0.5f);
98 INLINE static simdscalar vY(uint32_t sampleNum)
100 static const simdscalar Y = _simd_set1_ps(0.5f);
149 INLINE static simdscalar vX(uint32_t sampleNum)
154 INLINE static simdscalar vY(uint32_t sampleNum)
200 INLINE static simdscalar vX(uint32_t sampleNum)
202 static const simdscalar X[numSamples] {_simd_set1_ps(0.75f), _simd_set1_ps(0.25f)}
[all...] |
| frontend.h | 66 void triangleSetupABVertical(const simdscalar vX[3], const simdscalar vY[3], simdscalar (&vA)[3], simdscalar (&vB)[3])
207 simdscalar m00 = _simd_load1_ps(&vpMatrices.m00[0]);
208 simdscalar m30 = _simd_load1_ps(&vpMatrices.m30[0]);
209 simdscalar m11 = _simd_load1_ps(&vpMatrices.m11[0]);
210 simdscalar m31 = _simd_load1_ps(&vpMatrices.m31[0]);
211 simdscalar m22 = _simd_load1_ps(&vpMatrices.m22[0]);
212 simdscalar m32 = _simd_load1_ps(&vpMatrices.m32[0])
[all...] |
| format_conversion.h | 44 simdscalar vComp = _simd_load_ps((const float*)(pSrc + comp*sizeof(simdscalar)));
56 simdscalar vComp = FormatTraits<SrcFormat>::loadSOA(comp, pSrc);
82 INLINE simdscalar Clamp(simdscalar vComp, uint32_t Component)
128 INLINE simdscalar Normalize(simdscalar vComp, uint32_t Component)
151 simdscalar vComp = src.v[FormatTraits<DstFormat>::swizzle(comp)];
162 _simd_store_ps((float*)(pDst + comp*sizeof(simdscalar)), vComp);
169 simdscalar vComp = src.v[FormatTraits<DstFormat>::swizzle(comp)]
[all...] |
| backend.cpp | 160 simdscalar vComp;
430 simdmask ComputeUserClipMask(uint8_t clipMask, float* pUserClipBuffer, simdscalar vI, simdscalar vJ)
432 simdscalar vClipMask = _simd_setzero_ps();
438 simdscalar vA = _simd_broadcast_ss(pUserClipBuffer++);
439 simdscalar vB = _simd_broadcast_ss(pUserClipBuffer++);
440 simdscalar vC = _simd_broadcast_ss(pUserClipBuffer++);
443 simdscalar vInterp = vplaneps(vA, vB, vC, vI, vJ);
446 simdscalar vCull = _simd_cmp_ps(_simd_setzero_ps(), vInterp, _CMP_NLE_UQ);
478 const simdscalar dy = _simd_set1_ps(static_cast<float>(SIMD_TILE_Y_DIM))
[all...] |
| state.h | 268 simdscalar* pDomainU; // IN: (SIMD) Domain Point U coords
269 simdscalar* pDomainV; // IN: (SIMD) Domain Point V coords
271 simdscalar* pOutputData; // OUT: (SIMD) Vertex Attributes (2D array of vectors, one row per attribute-component)
291 simdscalar UL;
292 simdscalar center;
293 simdscalar sample;
294 simdscalar centroid;
307 simdscalar vZ; // INOUT: z location of pixels
309 simdscalar inputMask; // IN: input coverage mask for all samples
813 simdvector& vSrc, simdvector& vSrc1, simdscalar& vSrc0Alpha, uint32_t sample,
[all...] |
| pa.h | 133 // Assembles 1 primitive. Each simdscalar is a vertex (xyzw).
254 simdscalar tmp0 = _mm256_unpacklo_ps(a.x, a.z);
255 simdscalar tmp1 = _mm256_unpacklo_ps(a.y, a.w);
261 simdscalar tmp0 = _mm256_unpacklo_ps(a.x, a.z);
262 simdscalar tmp1 = _mm256_unpacklo_ps(a.y, a.w);
268 simdscalar tmp0 = _mm256_unpackhi_ps(a.x, a.z);
269 simdscalar tmp1 = _mm256_unpackhi_ps(a.y, a.w);
275 simdscalar tmp0 = _mm256_unpackhi_ps(a.x, a.z);
276 simdscalar tmp1 = _mm256_unpackhi_ps(a.y, a.w);
282 simdscalar tmp0 = _mm256_unpacklo_ps(a.x, a.z)
[all...] |
| backend.h | 44 simdmask ComputeUserClipMask(uint8_t clipMask, float* pUserClipBuffer, simdscalar vI, simdscalar vJ);
327 const simdscalar vXSamplePosUL, const simdscalar vYSamplePosUL)
401 const simdscalar vXSamplePosUL, const simdscalar vYSamplePosUL)
413 INLINE simdmask CalcDepthBoundsAcceptMask(simdscalar z, float minz, float maxz)
415 const simdscalar minzMask = _simd_cmpge_ps(z, _simd_set1_ps(minz));
416 const simdscalar maxzMask = _simd_cmple_ps(z, _simd_set1_ps(maxz));
554 uint32_t operator()(simdscalar& activeLanes, SWR_PS_CONTEXT& psContext,
[all...] |
| binner.cpp | 38 void BinPostSetupLines(DRAW_CONTEXT *pDC, PA_STATE& pa, uint32_t workerId, simdvector prims[3], simdscalar vRecipW[2], uint32_t primMask, simdscalari primID, simdscalari viewportIdx);
43 static const simdscalar g_pixelOffsets[SWR_PIXEL_LOCATION_UL + 1] =
53 INLINE simdscalari fpToFixedPointVertical(const simdscalar vIn)
55 simdscalar vFixed = _simd_mul_ps(vIn, _simd_set1_ps(PT::ScaleT::value));
454 simdscalar vRecipW0 = _simd_set1_ps(1.0f);
455 simdscalar vRecipW1 = _simd_set1_ps(1.0f);
456 simdscalar vRecipW2 = _simd_set1_ps(1.0f);
496 simdscalar offset = g_pixelOffsets[rastState.pixelLocation];
573 simdscalar recipW[2];
[all...] |
| tilemgr.cpp | 297 simdscalar valR = _simd_broadcast_ss(&pClearData[0]);
298 simdscalar valG = _simd_broadcast_ss(&pClearData[1]);
299 simdscalar valB = _simd_broadcast_ss(&pClearData[2]);
300 simdscalar valA = _simd_broadcast_ss(&pClearData[3]);
328 simdscalar valZ = _simd_broadcast_ss(&pClearData[0]);
|
| pa_avx.cpp | 205 simdscalar s;
341 simdscalar s;
345 simdscalar a0 = a[i];
346 simdscalar b0 = b[i];
454 simdscalar s;
459 simdscalar a0 = a[i];
460 simdscalar b0 = b[i];
519 simdscalar s1, s2;
523 simdscalar a0 = a[i];
524 simdscalar b0 = b[i]
[all...] |
| blend.h | 82 simdscalar oneMinusSrcA = _simd_sub_ps(_simd_set1_ps(1.0), src.w);
98 simdscalar oneMinusDstA = _simd_sub_ps(_simd_set1_ps(1.0), dst.w);
108 simdscalar sat = _simd_min_ps(src.w, _simd_sub_ps(_simd_set1_ps(1.0), dst.w));
|
| utils.h | 412 simdscalar src0 = _simd_load_ps((const float*)pSrc);
413 simdscalar src1 = _simd_load_ps((const float*)pSrc + 8);
414 simdscalar src2 = _simd_load_ps((const float*)pSrc + 16);
415 simdscalar src3 = _simd_load_ps((const float*)pSrc + 24);
464 simdscalar src0 = _simd_load_ps((const float*)pSrc);
465 simdscalar src1 = _simd_load_ps((const float*)pSrc + 8);
466 simdscalar src2 = _simd_load_ps((const float*)pSrc + 16);
708 simdscalar src = _simd_load_ps((const float*)pSrc);
[all...] |
| frontend.cpp | [all...] |
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/common/ |
| simdintrin.h | 36 typedef __m256 simdscalar; typedef
46 simdscalar v[4];
49 simdscalar x, y, z, w;
52 simdscalar& operator[] (const int i) { return v[i]; }
53 const simdscalar& operator[] (const int i) const { return v[i]; }
370 simdscalar vResult;
386 simdscalar vResult = vSrc;
640 simdscalari _simd_blendv_epi32(simdscalari a, simdscalari b, simdscalar mask)
653 simdscalar vMask(int32_t mask)
663 void _simd_mov(simdscalar &r, unsigned int rlane, simdscalar& s, unsigned int slane
[all...] |
| simd16intrin.h | 290 INLINE simdscalar _simd16_extract_ps(simd16scalar a, int imm8)
314 INLINE simd16scalar _simd16_insert_ps(simd16scalar a, simdscalar b, int imm8)
641 simdscalar lolo = _simd_permute_ps(a.lo, _simd_and_si(i.lo, mask));
642 simdscalar lohi = _simd_permute_ps(a.hi, _simd_and_si(i.lo, mask));
644 simdscalar hilo = _simd_permute_ps(a.lo, _simd_and_si(i.hi, mask));
645 simdscalar hihi = _simd_permute_ps(a.hi, _simd_and_si(i.hi, mask));
[all...] |
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/ |
| StoreTile.h | 694 static const uint32_t offset = sizeof(simdscalar);
697 simdscalar vComp0 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(0))*offset)); // float32 rrrrrrrr
698 simdscalar vComp1 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(1))*offset)); // float32 gggggggg
699 simdscalar vComp2 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(2))*offset)); // float32 bbbbbbbb
700 simdscalar vComp3 = _simd_load_ps((const float*)(pSrc + (FormatTraits<DstFormat>::swizzle(3))*offset)); // float32 aaaaaaaa
[all...] |
