fdo-mirrors/mesa
1
0
Fork 0
mirror of https://gitlab.freedesktop.org/mesa/mesa.git synced 2026-05-02 14:28:05 +02:00
Code Issues Projects Releases Packages Wiki Activity Actions 1

swr/rast: Faster emulated simd16 permute

Browse source 
Speed up simd16 frontend (default) on avx/avx2 platforms;
fixes performance regression caused by switch to simdlib.

Reviewed-by: Bruce Cherniak <bruce.cherniak@intel.com>
Cc: mesa-stable@lists.freedesktop.org
(cherry picked from commit d8489517a5)
This commit is contained in:
Tim Rowley 2017-11-13 18:39:38 -06:00 • committed by Emil Velikov
parent c798200543
commit 957c66de1c
1 changed files with 11 additions and 23 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

34
src/gallium/drivers/swr/rasterizer/common/simdlib_512_emu.inl
View file

@ -521,36 +521,24 @@ SIMD_IWRAPPER_2(packus_epi32); // See documentation for _mm256_packus_epi32
static SIMDINLINE Integer SIMDCALL permute_epi32(Integer const &a, Integer const &swiz) // return a[swiz[i]] for each 32-bit lane i (int32)
{
Integer result;
// Ugly slow implementation
uint32_t const *pA = reinterpret_cast<uint32_t const*>(&a);
uint32_t const *pSwiz = reinterpret_cast<uint32_t const*>(&swiz);
uint32_t *pResult = reinterpret_cast<uint32_t *>(&result);
for (uint32_t i = 0; i < SIMD_WIDTH; ++i)
{
pResult[i] = pA[0xF & pSwiz[i]];
}
return result;
return castps_si(permute_ps(castsi_ps(a), swiz));
}
static SIMDINLINE Float SIMDCALL permute_ps(Float const &a, Integer const &swiz) // return a[swiz[i]] for each 32-bit lane i (float)
{
Float result;
const auto mask = SIMD256T::set1_epi32(7);
// Ugly slow implementation
float const *pA = reinterpret_cast<float const*>(&a);
uint32_t const *pSwiz = reinterpret_cast<uint32_t const*>(&swiz);
float *pResult = reinterpret_cast<float *>(&result);
auto lolo = SIMD256T::permute_ps(a.v8[0], SIMD256T::and_si(swiz.v8[0], mask));
auto lohi = SIMD256T::permute_ps(a.v8[1], SIMD256T::and_si(swiz.v8[0], mask));
for (uint32_t i = 0; i < SIMD_WIDTH; ++i)
auto hilo = SIMD256T::permute_ps(a.v8[0], SIMD256T::and_si(swiz.v8[1], mask));
auto hihi = SIMD256T::permute_ps(a.v8[1], SIMD256T::and_si(swiz.v8[1], mask));
return Float
{
pResult[i] = pA[0xF & pSwiz[i]];
}
return result;
SIMD256T::blendv_ps(lolo, lohi, SIMD256T::castsi_ps(SIMD256T::cmpgt_epi32(swiz.v8[0], mask))),
SIMD256T::blendv_ps(hilo, hihi, SIMD256T::castsi_ps(SIMD256T::cmpgt_epi32(swiz.v8[1], mask))),
};
}
// All of the 512-bit permute2f128_XX intrinsics do the following: