| /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/swr/rasterizer/common/ |
| simdlib_128_avx2.inl | 41 static SIMDINLINE Integer SIMDCALL sllv_epi32(Integer vA, Integer vB) // return a << b (uint32)
43 return _mm_sllv_epi32(vA, vB);
46 static SIMDINLINE Integer SIMDCALL srlv_epi32(Integer vA, Integer vB) // return a >> b (uint32)
48 return _mm_srlv_epi32(vA, vB);
|
| simdlib_128_avx.inl | 163 static SIMDINLINE Integer SIMDCALL sllv_epi32(Integer vA, Integer vB) // return a << b (uint32)
166 a = _mm_extract_epi32(vA, 0);
169 vA = _mm_insert_epi32(vA, a, 0);
171 a = _mm_extract_epi32(vA, 1);
174 vA = _mm_insert_epi32(vA, a, 1);
176 a = _mm_extract_epi32(vA, 2);
179 vA = _mm_insert_epi32(vA, a, 2)
[all...] |
| simdintrin.h | 195 /// @brief Compute plane equation vA * vX + vB * vY + vC
196 SIMDINLINE simdscalar vplaneps(simdscalar const& vA,
202 simdscalar vOut = _simd_fmadd_ps(vA, vX, vC);
208 /// @brief Compute plane equation vA * vX + vB * vY + vC
209 SIMDINLINE simd4scalar vplaneps(simd4scalar const& vA,
215 simd4scalar vOut = _simd128_fmadd_ps(vA, vX, vC);
241 simdscalar vA = _simd_broadcast_ss(pInterpA);
248 return vplaneps(vA, vB, vC, vI, vJ);
259 simdscalar vA = _simd_broadcast_ss(pInterpA);
261 return vA;
[all...] |
| simdlib_256_avx.inl | 239 static SIMDINLINE Integer SIMDCALL sllv_epi32(Integer const& vA,
243 __m128i vAHi = _mm_castps_si128(_mm256_extractf128_ps(_mm256_castsi256_ps(vA), 1));
244 __m128i vALow = _mm_castps_si128(_mm256_extractf128_ps(_mm256_castsi256_ps(vA), 0));
304 static SIMDINLINE Integer SIMDCALL srlv_epi32(Integer const& vA,
308 __m128i vAHi = _mm_castps_si128(_mm256_extractf128_ps(_mm256_castsi256_ps(vA), 1));
309 __m128i vALow = _mm_castps_si128(_mm256_extractf128_ps(_mm256_castsi256_ps(vA), 0));
|
| /xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/swr/rasterizer/common/ |
| simdlib_128_avx2.inl | 41 static SIMDINLINE Integer SIMDCALL sllv_epi32(Integer vA, Integer vB) // return a << b (uint32)
43 return _mm_sllv_epi32(vA, vB);
46 static SIMDINLINE Integer SIMDCALL srlv_epi32(Integer vA, Integer vB) // return a >> b (uint32)
48 return _mm_srlv_epi32(vA, vB);
|
| simdlib_128_avx.inl | 163 static SIMDINLINE Integer SIMDCALL sllv_epi32(Integer vA, Integer vB) // return a << b (uint32)
166 a = _mm_extract_epi32(vA, 0);
169 vA = _mm_insert_epi32(vA, a, 0);
171 a = _mm_extract_epi32(vA, 1);
174 vA = _mm_insert_epi32(vA, a, 1);
176 a = _mm_extract_epi32(vA, 2);
179 vA = _mm_insert_epi32(vA, a, 2)
[all...] |
| simdintrin.h | 246 /// @brief Compute plane equation vA * vX + vB * vY + vC
247 SIMDINLINE simdscalar vplaneps(simdscalar const& vA,
253 simdscalar vOut = _simd_fmadd_ps(vA, vX, vC);
259 /// @brief Compute plane equation vA * vX + vB * vY + vC
260 SIMDINLINE simd4scalar vplaneps(simd4scalar const& vA,
266 simd4scalar vOut = _simd128_fmadd_ps(vA, vX, vC);
285 simdscalar vA = _simd_broadcast_ss(pInterpA);
292 return vplaneps(vA, vB, vC, vI, vJ);
303 simdscalar vA = _simd_broadcast_ss(pInterpA);
305 return vA;
[all...] |
| simdlib_256_avx.inl | 239 static SIMDINLINE Integer SIMDCALL sllv_epi32(Integer const& vA,
243 __m128i vAHi = _mm_castps_si128(_mm256_extractf128_ps(_mm256_castsi256_ps(vA), 1));
244 __m128i vALow = _mm_castps_si128(_mm256_extractf128_ps(_mm256_castsi256_ps(vA), 0));
304 static SIMDINLINE Integer SIMDCALL srlv_epi32(Integer const& vA,
308 __m128i vAHi = _mm_castps_si128(_mm256_extractf128_ps(_mm256_castsi256_ps(vA), 1));
309 __m128i vALow = _mm_castps_si128(_mm256_extractf128_ps(_mm256_castsi256_ps(vA), 0));
|
| /xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/swr/rasterizer/core/core/ |
| frontend.h | 43 void triangleSetupAB(const __m128 vX, const __m128 vY, __m128& vA, __m128& vB)
48 vA = _mm_sub_ps(vY, vYsub);
67 void triangleSetupABInt(const __m128i vX, const __m128i vY, __m128i& vA, __m128i& vB)
74 vA = _mm_sub_epi32(vY, vYsub);
83 simdscalari (&vA)[3],
88 vA[0] = _simd_sub_epi32(vY[0], vY[1]);
89 vA[1] = _simd_sub_epi32(vY[1], vY[2]);
90 vA[2] = _simd_sub_epi32(vY[2], vY[0]);
101 simd16scalari (&vA)[3],
106 vA[0] = _simd16_sub_epi32(vY[0], vY[1])
[all...] |
| rasterizer_impl.h | 102 /// @param vA, vB - A & B coefs for each edge of the triangle (Ax + Bx + C)
277 INLINE void adjustTopLeftRuleIntFix16(const __m128i vA, const __m128i vB, __m256d& vEdge)
279 // if vA < 0, vC--
280 // if vA == 0 && vB < 0, vC--
285 // if vA < 0 (line is not horizontal and below)
286 int msk = _mm_movemask_ps(_mm_castsi128_ps(vA));
288 // if vA == 0 && vB < 0 (line is horizontal and we're on the left edge of a tri)
289 __m128i vCmp = _mm_cmpeq_epi32(vA, _mm_setzero_si128());
961 __m128 vA, vB;
962 triangleSetupAB(vX, vY, vA, vB)
[all...] |
| backend_impl.h | 66 simdscalar vA = _simd_broadcast_ss(pUserClipBuffer++);
71 simdscalar vInterp = vplaneps(vA, vB, vC, vI, vJ);
|
| /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/llvmpipe/ |
| lp_setup_analysis.c | 184 * vA + +--------------------------------------------+ + vC
211 * rectangles by introducing new vertices at vA, vB, vC and vD, and
242 PIPE_ALIGN_VAR(16) float vA[2][4];
286 make_vert(v18, v9, vA);
291 assert(test_interps((const_float4_ptr)vA, as, bs, at, bt));
299 (const_float4_ptr)vA);
|
| /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/swr/rasterizer/jitter/ |
| builder_misc.h | 115 Value* VRCP(Value* va, const llvm::Twine& name = "");
116 Value* VPLANEPS(Value* vA, Value* vB, Value* vC, Value*& vX, Value*& vY);
|
| builder_misc.cpp | 351 Value* Builder::VRCP(Value* va, const llvm::Twine& name)
353 return FDIV(VIMMED1(1.0f), va, name); // 1 / a
356 Value* Builder::VPLANEPS(Value* vA, Value* vB, Value* vC, Value*& vX, Value*& vY)
358 Value* vOut = FMADDPS(vA, vX, vC);
|
| /xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/swr/rasterizer/jitter/ |
| builder_misc.h | 101 Value* VRCP(Value* va, const llvm::Twine& name = "");
102 Value* VPLANEPS(Value* vA, Value* vB, Value* vC, Value*& vX, Value*& vY);
|
| builder_misc.cpp | 300 Value* Builder::VRCP(Value* va, const llvm::Twine& name)
302 return FDIV(VIMMED1(1.0f), va, name); // 1 / a
305 Value* Builder::VPLANEPS(Value* vA, Value* vB, Value* vC, Value*& vX, Value*& vY)
307 Value* vOut = FMADDPS(vA, vX, vC);
|
| /xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/nouveau/codegen/ |
| nv50_ir_ra.cpp | 1368 const LValue *vA = node->getValue();
1373 if (vA->compound | vB->compound) {
1375 for (Value::DefCIterator D = vA->defs.begin(); D != vA->defs.end(); ++D) {
1408 vA->id, vB->id, intf->reg, intf->colors);
|
| /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/nouveau/codegen/ |
| nv50_ir_ra.cpp | 1417 LValue *vA = node->getValue();
1422 if (vA->compound | vB->compound) {
1424 for (const ValueDef *D : mergedDefs(vA)) {
1457 vA->id, vB->id, intf->reg, intf->colors);
|
