Skip to content

Add AVX512 accelerated 1D/3D LUTS #1932

New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

Sign up for GitHub

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Merged
doug-walker merged 9 commits into from
Mar 21, 2024
Merged

Add AVX512 accelerated 1D/3D LUTS #1932

Show file tree
Hide file tree
Changes from all commits
Commits
Show all changes
9 commits
Select commit Hold shift + click to select a range
4f6f8d7
Initial AVX512 support
markreidvfx Jan 13, 2024
49f9ee4
Lut1DOp add AVX512 implementation
markreidvfx Jan 13, 2024
f35b33a
Lut3DOp add AVX512 implementation
markreidvfx Jan 13, 2024
916f133
Don't use SIMD if only 1 pixel is requested
markreidvfx Jan 13, 2024
0c7ee25
Remove #if, f16c is always available with AVX512
markreidvfx Jan 28, 2024
3a69085
Cast pointers to __m512 instead of __m256
markreidvfx Jan 28, 2024
ce3fcbd
Use size method from vector being tested
markreidvfx Jan 28, 2024
15a41f9
Add to help message that f16c is only used with AVX/AVX2
markreidvfx Jan 28, 2024
3e33b9c
Clarify test case by using uint8 maxValue
markreidvfx Mar 20, 2024
File filter

Filter by extension

Filter by extension
Conversations
Failed to load comments.
Loading
Jump to
Jump to file
Failed to load files.
Loading
Diff view
Diff view
4 changes: 3 additions & 1 deletion share/cmake/utils/CheckSupportAVX512.cmake
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -5,7 +5,7 @@ include(CheckCXXSourceCompiles)

set(_cmake_cxx_flags_orig "${CMAKE_CXX_FLAGS}")

if(APPLE AND ("${CMAKE_OSX_ARCHITECTURES}" MATCHES "arm64;x86_64"
if(APPLE AND ("${CMAKE_OSX_ARCHITECTURES}" MATCHES "arm64;x86_64"
OR "${CMAKE_OSX_ARCHITECTURES}" MATCHES "x86_64;arm64"))
set(__universal_build 1)
set(_cmake_osx_architectures_orig "${CMAKE_OSX_ARCHITECTURES}")
Expand All @@ -28,6 +28,8 @@ set(AVX512_CODE "

int main() {
__m512i vec = _mm512_set1_epi32(42);
// gcc <= 6 appear to be missing this intrinsic
__mmask16 k = _mm512_int2mask(42);
return 0;
}
")
Expand Down
8 changes: 8 additions & 0 deletions share/cmake/utils/CheckSupportX86SIMD.cmake
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -31,6 +31,10 @@ if(MSVC)
if (COMPILER_SUPPORTS_AVX2)
set(OCIO_AVX2_ARGS "/arch:AVX2")
endif()

if (COMPILER_SUPPORTS_AVX512)
set(OCIO_AVX512_ARGS "/arch:AVX512")
endif()
else()
if (COMPILER_SUPPORTS_SSE2)
set(OCIO_SSE2_ARGS "-msse2")
Expand All @@ -42,6 +46,10 @@ else()

if (COMPILER_SUPPORTS_AVX2)
set(OCIO_AVX2_ARGS "-mavx2" "-mfma")
endif()

if (COMPILER_SUPPORTS_AVX512)
set(OCIO_AVX512_ARGS "-mavx512f")
endif()
endif()

Expand Down
Loading