Code/UnitTests/FoundationTest/SimdMath/SimdVec4bWideTest.cpp - dev - redgpu/ezEngine

Code/UnitTests/FoundationTest/SimdMath/SimdVec4bWideTest.cpp
147 строк5 KB
Trevor Cash
ezSimdVec4d-SSE (re-open) (#1735)
05 янв 2026, 11:52
05 янв 2026, 11:523b2f02a
#include <FoundationTest/FoundationTestPCH.h>

#include <Foundation/SimdMath/SimdVec4b_Wide.h>

EZ_CREATE_SIMPLE_TEST(SimdMath, SimdVec4bWide)
{
  EZ_TEST_BLOCK(ezTestBlock::Enabled, "Constructor")
  {
#if EZ_DISABLED(EZ_COMPILER_GCC) && EZ_DISABLED(EZ_COMPILE_FOR_DEBUG)
    // Placement new of the default constructor should not have any effect on the previous data.
    alignas(16) double testBlock[4] = {1, 2, 3, 4};
    ezSimdVec4bWide* pDefCtor = ::new ((void*)&testBlock[0]) ezSimdVec4bWide;
    EZ_TEST_BOOL(testBlock[0] == 1.0 && testBlock[1] == 2.0 && testBlock[2] == 3.0 && testBlock[3] == 4.0);
#endif

    // Make sure the class didn't accidentally change in size.
#if EZ_SSE_LEVEL >= EZ_SSE_AVX
    static_assert(sizeof(ezSimdVec4bWide) == 32);
    static_assert(alignof(ezSimdVec4bWide) == 32);
#else

    static_assert(sizeof(ezSimdVec4bWide) == 32);

#if EZ_SIMD_IMPLEMENTATION == EZ_SIMD_IMPLEMENTATION_SSE
    static_assert(alignof(ezSimdVec4bWide) == 16);
#elif EZ_SIMD_IMPLEMENTATION == EZ_SIMD_IMPLEMENTATION_FPU
    static_assert(alignof(ezSimdVec4bWide) == 8);
#endif

    #endif

    ezSimdVec4bWide vInit1B(true);
    EZ_TEST_BOOL(vInit1B.x() == true && vInit1B.y() == true && vInit1B.z() == true && vInit1B.w() == true);

    // Make sure all components have the correct value
#if EZ_SSE_LEVEL >= EZ_SSE_AVX
    alignas(32) ezUInt64 vals[4];
    _mm256_store_si256((__m256i*)vals, _mm256_castpd_si256(vInit1B.m_v));

    EZ_TEST_BOOL(vals[0] == 0xFFFFFFFFFFFFFFFFULL
      && vals[1] == 0xFFFFFFFFFFFFFFFFULL
      && vals[2] == 0xFFFFFFFFFFFFFFFFULL
      && vals[3] == 0xFFFFFFFFFFFFFFFFULL);
#else

#if EZ_SIMD_IMPLEMENTATION == EZ_SIMD_IMPLEMENTATION_SSE
    alignas(16) ezUInt64 valsXY[2];
    alignas(16) ezUInt64 valsZW[2];
    _mm_store_si128((__m128i*)valsXY, _mm_castpd_si128(vInit1B.m_v.xy));
    _mm_store_si128((__m128i*)valsZW, _mm_castpd_si128(vInit1B.m_v.zw));

    EZ_TEST_BOOL(valsXY[0] == 0xFFFFFFFFFFFFFFFFULL
      && valsXY[1] == 0xFFFFFFFFFFFFFFFFULL
      && valsZW[0] == 0xFFFFFFFFFFFFFFFFULL
      && valsZW[1] == 0xFFFFFFFFFFFFFFFFULL);
#endif

#endif

    ezSimdVec4bWide vInit4B(false, true, false, true);
    EZ_TEST_BOOL(vInit4B.x() == false && vInit4B.y() == true && vInit4B.z() == false && vInit4B.w() == true);

    // Make sure all components have the correct value
#if EZ_SSE_LEVEL >= EZ_SSE_AVX
    _mm256_store_si256((__m256i*)vals, _mm256_castpd_si256(vInit4B.m_v));
    EZ_TEST_BOOL(vals[0] == 0
      && vals[1] == 0xFFFFFFFFFFFFFFFFULL
      && vals[2] == 0
      && vals[3] == 0xFFFFFFFFFFFFFFFFULL);
#else

#if EZ_SIMD_IMPLEMENTATION == EZ_SIMD_IMPLEMENTATION_SSE
    _mm_store_si128((__m128i*)valsXY, _mm_castpd_si128(vInit4B.m_v.xy));
    _mm_store_si128((__m128i*)valsZW, _mm_castpd_si128(vInit4B.m_v.zw));
    
    EZ_TEST_BOOL(valsXY[0] == 0
      && valsXY[1] == 0xFFFFFFFFFFFFFFFFULL
      && valsZW[0] == 0
      && valsZW[1] == 0xFFFFFFFFFFFFFFFFULL);
#endif
#endif

    ezSimdVec4bWide vCopy(vInit4B);
    EZ_TEST_BOOL(vCopy.x() == false && vCopy.y() == true && vCopy.z() == false && vCopy.w() == true);

    EZ_TEST_BOOL(
      vCopy.GetComponent<0>() == false && vCopy.GetComponent<1>() == true && vCopy.GetComponent<2>() == false && vCopy.GetComponent<3>() == true);
  }

  EZ_TEST_BLOCK(ezTestBlock::Enabled, "Swizzle")
  {
    ezSimdVec4bWide a(true, false, true, false);

    ezSimdVec4bWide b = a.Get<ezSwizzle::XXXX>();
    EZ_TEST_BOOL(b.x() && b.y() && b.z() && b.w());

    b = a.Get<ezSwizzle::YYYX>();
    EZ_TEST_BOOL(!b.x() && !b.y() && !b.z() && b.w());

    b = a.Get<ezSwizzle::ZZZX>();
    EZ_TEST_BOOL(b.x() && b.y() && b.z() && b.w());

    b = a.Get<ezSwizzle::WWWX>();
    EZ_TEST_BOOL(!b.x() && !b.y() && !b.z() && b.w());
  }

  EZ_TEST_BLOCK(ezTestBlock::Enabled, "Operators")
  {
    ezSimdVec4bWide a(true, false, true, false);
    ezSimdVec4bWide b(false, true, true, false);

    ezSimdVec4bWide c = a && b;
    EZ_TEST_BOOL(!c.x() && !c.y() && c.z() && !c.w());

    c = a || b;
    EZ_TEST_BOOL(c.x() && c.y() && c.z() && !c.w());

    c = !a;
    EZ_TEST_BOOL(!c.x() && c.y() && !c.z() && c.w());
    EZ_TEST_BOOL(c.AnySet<2>());
    EZ_TEST_BOOL(!c.AllSet<4>());
    EZ_TEST_BOOL(!c.NoneSet<4>());

    c = c || a;
    EZ_TEST_BOOL(c.AnySet<4>());
    EZ_TEST_BOOL(c.AllSet<4>());
    EZ_TEST_BOOL(!c.NoneSet<4>());

    c = !c;
    EZ_TEST_BOOL(!c.AnySet<4>());
    EZ_TEST_BOOL(!c.AllSet<4>());
    EZ_TEST_BOOL(c.NoneSet<4>());

    c = a == b;
    EZ_TEST_BOOL(!c.x() && !c.y() && c.z() && c.w());

    c = a != b;
    EZ_TEST_BOOL(c.x() && c.y() && !c.z() && !c.w());

    EZ_TEST_BOOL(a.AllSet<1>());
    EZ_TEST_BOOL(b.NoneSet<1>());

    ezSimdVec4bWide cmp(false, true, false, true);
    c = ezSimdVec4bWide::Select(cmp, a, b);
    EZ_TEST_BOOL(!c.x() && !c.y() && c.z() && !c.w());
  }
}