| /external/mesa3d/src/gallium/drivers/swr/rasterizer/core/ |
| frontend.h | 95 void triangleSetupABIntVertical(const simdscalari vX[3], const simdscalari vY[3], simdscalari (&vA)[3], simdscalari (&vB)[3])
145 void calcDeterminantIntVertical(const simdscalari vA[3], const simdscalari vB[3], simdscalari *pvDet)
149 simdscalari vA1Lo = _simd_unpacklo_epi32(vA[1], vA[1]); // 0 0 1 1 4 4 5 5
150 simdscalari vA1Hi = _simd_unpackhi_epi32(vA[1], vA[1]); // 2 2 3 3 6 6 7 7
152 simdscalari vB2Lo = _simd_unpacklo_epi32(vB[2], vB[2])
[all...] |
| utils.h | 80 simdscalari ymin;
81 simdscalari ymax;
82 simdscalari xmin;
83 simdscalari xmax;
291 simdscalari src = _simd_load_si((const simdscalari*)pSrc);
306 simdscalari dst01 = _mm256_shuffle_epi8(src,
308 simdscalari dst23 = _mm256_permute2x128_si256(src, src, 0x01);
311 simdscalari dst = _mm256_or_si256(dst01, dst23);
312 _simd_store_si((simdscalari*)pDst, dst)
[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);
53 INLINE simdscalari fpToFixedPointVertical(const simdscalar vIn)
65 INLINE static void FPToFixedPoint(const simdvector * const tri, simdscalari(&vXi)[3], simdscalari(&vYi)[3])
84 INLINE void calcBoundingBoxIntVertical(const simdvector * const tri, simdscalari(&vX)[3], simdscalari(&vY)[3], simdBBox &bbox)
86 simdscalari vMinX = vX[0];
90 simdscalari vMaxX = vX[0];
94 simdscalari vMinY = vY[0]
[all...] |
| clip.h | 66 void ComputeClipCodes(const API_STATE& state, const simdvector& vertex, simdscalar& clipCodes, simdscalari viewportIndexes)
143 void ComputeClipCodes(simdvector vertex[], simdscalari viewportIndexes)
266 void ClipSimd(const simdscalar& vPrimMask, const simdscalar& vClipMask, PA_STATE& pa, const simdscalari& vPrimId, const simdscalari& vViewportIdx)
339 simdscalari vNumClippedVerts = ClipPrims((float*)&vertices[0], vPrimMask, vClipMask, numAttribs);
368 const simdscalari vOffsets = _mm256_set_epi32(
463 void ExecuteStage(PA_STATE& pa, simdvector prim[], uint32_t primMask, simdscalari primId, simdscalari viewportIdx)
537 inline simdscalari ComputeOffsets(uint32_t attrib, simdscalari vIndices, uint32_t component
[all...] |
| multisample.h | 72 INLINE static simdscalari FullSampleMask() = delete;
125 INLINE static simdscalari FullSampleMask(){return _simd_set1_epi32(0x1);};
174 INLINE static simdscalari FullSampleMask(){return _simd_set1_epi32(0x1);};
235 INLINE static simdscalari FullSampleMask()
237 static const simdscalari mask =_simd_set1_epi32(0x3);
288 INLINE static simdscalari FullSampleMask()
290 static const simdscalari mask =_simd_set1_epi32(0x3);
356 INLINE static simdscalari FullSampleMask()
358 static const simdscalari mask = _simd_set1_epi32(0xF);
409 INLINE static simdscalari FullSampleMask(
[all...] |
| format_types.h | 123 simdscalari src = _simd_castps_si(in);
163 simdscalari inlo = _simd_castps_si(_simd16_extract_ps(in, 0)); // r0 r1 r2 r3 r4 r5 r6 r7 (32b)
164 simdscalari inhi = _simd_castps_si(_simd16_extract_ps(in, 1)); // r8 r9 rA rB rC rD rE rF
166 simdscalari permlo = _simd_permute2f128_si(inlo, inhi, 0x20); // r0 r1 r2 r3 r8 r9 rA rB (32b)
167 simdscalari permhi = _simd_permute2f128_si(inlo, inhi, 0x31); // r4 r5 r6 r7 rC rD rE rF (32b)
169 simdscalari pack = _simd_packus_epi32(permlo, permhi); // r0 r1 r2 r3 r4 r5 r6 r7 r8 r9 rA rB rC rD rE rF (16b)
171 const simdscalari zero = _simd_setzero_si();
238 simdscalari src = _simd_castps_si(in);
278 simdscalari inlo = _simd_castps_si(_simd16_extract_ps(in, 0)); // r0 r1 r2 r3 r4 r5 r6 r7 (32b)
279 simdscalari inhi = _simd_castps_si(_simd16_extract_ps(in, 1)); // r8 r9 rA rB rC rD rE r
[all...] |
| clip.cpp | 182 void ClipTriangles(DRAW_CONTEXT *pDC, PA_STATE& pa, uint32_t workerId, simdvector prims[], uint32_t primMask, simdscalari primId, simdscalari viewportIdx)
191 void ClipLines(DRAW_CONTEXT *pDC, PA_STATE& pa, uint32_t workerId, simdvector prims[], uint32_t primMask, simdscalari primId, simdscalari viewportIdx)
199 void ClipPoints(DRAW_CONTEXT *pDC, PA_STATE& pa, uint32_t workerId, simdvector prims[], uint32_t primMask, simdscalari primId, simdscalari viewportIdx)
|
| state.h | 205 simdscalari VertexID; // IN: Vertex ID
206 simdscalari mask; // IN: Active mask for shader
252 simdscalari PrimitiveID; // IN: (SIMD) primitive ID generated from the draw call
253 simdscalari mask; // IN: Active mask for shader
270 simdscalari mask; // IN: Active mask for shader
281 simdscalari PrimitiveID; // IN: input primitive ID generated from the draw call
283 simdscalari mask; // IN: Active mask for shader
286 simdscalari vertexCount; // OUT: num vertices emitted per SIMD lane
308 simdscalari activeMask; // OUT: mask for kill
310 simdscalari oMask; // OUT: mask for output coverag
[all...] |
| depthstencil.h | 35 simdscalari stencil = _simd_castps_si(stencilps);
49 simdscalari stencilincr = _simd_adds_epu8(stencil, _simd_set1_epi32(1));
55 simdscalari stencildecr = _simd_subs_epu8(stencil, _simd_set1_epi32(1));
61 simdscalari stencilincr = _simd_add_epi8(stencil, _simd_set1_epi32(1));
67 simdscalari stencildecr = _simd_add_epi8(stencil, _simd_set1_epi32((-1) & 0xff));
274 simdscalari vWriteMask = _simd_set1_epi32(stencilWriteMask);
|
| pa.h | 58 virtual simdscalari GetPrimID(uint32_t startID) = 0;
93 simdscalari primID;
231 simdscalari GetPrimID(uint32_t startID)
342 simdscalari vOffsets[MAX_NUM_VERTS_PER_PRIM]; // byte offsets for currently assembling simd
348 simdscalari vPrimId; // vector of prim ID
442 simdscalari GetPrimID(uint32_t startID)
548 simdscalari vIndices = *(simdscalari*)&this->indices[v][0];
552 simdscalari vVertexBatch = _simd_srai_epi32(vIndices, simdShift);
557 simdscalari vVertexIndex = _simd_and_si(vIndices, _simd_set1_epi32(simdMask))
[all...] |
| tilemgr.cpp | 351 simdscalari valS = _simd_set1_epi8(clearVal);
353 simdscalari* pBuf = (simdscalari*)pHotTile->pBuffer;
|
| context.h | 218 uint32_t primMask, simdscalari primID, simdscalari viewportIdx);
|
| format_conversion.h | 103 simdscalari vCompi = _simd_castps_si(vComp);
112 simdscalari vCompi = _simd_castps_si(vComp);
|
| frontend.cpp | 480 static INLINE simdscalari GenerateMask(uint32_t numItemsRemaining)
656 simdscalari primID)
812 simdscalari vPrimId;
826 simdscalari vViewPortIdx;
833 simdscalari vNumViewports = _simd_set1_epi32(KNOB_NUM_VIEWPORTS_SCISSORS);
834 simdscalari vClearMask = _simd_cmplt_epi32(_simd_castps_si(vpiAttrib[0].x), vNumViewports);
[all...] |
| pa_avx.cpp | 246 const simdscalari perm0 = _simd_set_epi32(5, 2, 7, 4, 1, 6, 3, 0);
247 const simdscalari perm1 = _simd_set_epi32(6, 3, 0, 5, 2, 7, 4, 1);
248 const simdscalari perm2 = _simd_set_epi32(7, 4, 1, 6, 3, 0, 5, 2);
[all...] |
| backend.h | [all...] |
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/common/ |
| simdintrin.h | 37 typedef __m256i simdscalari; typedef
624 simdscalari _simd_loadu2_si(const __m128i *hiaddr, const __m128i *loaddr)
633 void _simd_storeu2_si(__m128i *hiaddr, __m128i *loaddr, simdscalari a)
640 simdscalari _simd_blendv_epi32(simdscalari a, simdscalari b, simdscalar mask)
646 simdscalari _simd_blendv_epi32(simdscalari a, simdscalari b, simdscalari mask
[all...] |
| simd16intrin.h | 302 INLINE simdscalari _simd16_extract_si(simd16scalari a, int imm8)
328 INLINE simd16scalari _simd16_insert_si(simd16scalari a, simdscalari b, int imm8)
639 const simdscalari mask = _simd_set1_epi32(7);
742 INLINE simd16scalari _simd16_cvtepu8_epi16(simdscalari a)
762 INLINE simd16scalari _simd16_cvtepu16_epi32(simdscalari a)
[all...] |
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/ |
| StoreTile.h | 511 simdscalari packed = _simd_castps_si(dst.x);
566 simdscalari destlo = _simd_loadu2_si(reinterpret_cast<__m128i *>(ppDsts[1]), reinterpret_cast<__m128i *>(ppDsts[0]));
567 simdscalari desthi = _simd_loadu2_si(reinterpret_cast<__m128i *>(ppDsts[3]), reinterpret_cast<__m128i *>(ppDsts[2]));
[all...] |
