wehub-resource-sync
143 lines
3.2 KiB
CMake
143 lines
3.2 KiB
CMake
# This file is use to check all support level of AVX on your machine
|
|
# so that PaddlePaddle can unleash the vectorization power of multicore.
|
|
|
|
include(CheckCXXSourceRuns)
|
|
include(CheckCXXSourceCompiles)
|
|
|
|
if(CMAKE_CXX_COMPILER_ID MATCHES "GNU|Clang")
|
|
set(MMX_FLAG "-mmmx")
|
|
set(SSE2_FLAG "-msse2")
|
|
set(SSE3_FLAG "-msse3")
|
|
set(AVX_FLAG "-mavx")
|
|
set(AVX2_FLAG "-mavx2")
|
|
set(AVX512F_FLAG "-mavx512f")
|
|
set(Wno_Maybe_Uninitialized "-Wno-maybe-uninitialized")
|
|
set(FMA_FLAG "-mfma")
|
|
if(${CMAKE_CXX_COMPILER_VERSION} VERSION_GREATER_EQUAL 11.0)
|
|
set(NO_INLINE "-fno-inline")
|
|
else()
|
|
set(NO_INLINE "")
|
|
endif()
|
|
elseif(MSVC)
|
|
set(MMX_FLAG "/arch:MMX")
|
|
set(SSE2_FLAG "/arch:SSE2")
|
|
set(SSE3_FLAG "/arch:SSE3")
|
|
set(AVX_FLAG "/arch:AVX")
|
|
set(AVX2_FLAG "/arch:AVX2")
|
|
set(AVX512F_FLAG "/arch:AVX512")
|
|
set(Wno_Maybe_Uninitialized "/wd4701")
|
|
set(FMA_FLAG "/arch:AVX2")
|
|
if(${CMAKE_CXX_COMPILER_VERSION} VERSION_GREATER_EQUAL 11.0)
|
|
set(NO_INLINE "/Ob0")
|
|
else()
|
|
set(NO_INLINE "")
|
|
endif()
|
|
endif()
|
|
|
|
set(CMAKE_REQUIRED_FLAGS_RETAINED ${CMAKE_REQUIRED_FLAGS})
|
|
|
|
# Check MMX
|
|
set(CMAKE_REQUIRED_FLAGS ${MMX_FLAG})
|
|
set(MMX_FOUND_EXITCODE
|
|
1
|
|
CACHE STRING "Result from TRY_RUN" FORCE)
|
|
check_cxx_source_runs(
|
|
"
|
|
#include <mmintrin.h>
|
|
int main()
|
|
{
|
|
_mm_setzero_si64();
|
|
return 0;
|
|
}"
|
|
MMX_FOUND)
|
|
|
|
# Check SSE2
|
|
set(CMAKE_REQUIRED_FLAGS ${SSE2_FLAG})
|
|
set(SSE2_FOUND_EXITCODE
|
|
1
|
|
CACHE STRING "Result from TRY_RUN" FORCE)
|
|
check_cxx_source_runs(
|
|
"
|
|
#include <emmintrin.h>
|
|
int main()
|
|
{
|
|
_mm_setzero_si128();
|
|
return 0;
|
|
}"
|
|
SSE2_FOUND)
|
|
|
|
# Check SSE3
|
|
set(CMAKE_REQUIRED_FLAGS ${SSE3_FLAG})
|
|
set(SSE3_FOUND_EXITCODE
|
|
1
|
|
CACHE STRING "Result from TRY_RUN" FORCE)
|
|
check_cxx_source_runs(
|
|
"
|
|
#include <pmmintrin.h>
|
|
int main()
|
|
{
|
|
__m128d a = _mm_set1_pd(6.28);
|
|
__m128d b = _mm_set1_pd(3.14);
|
|
__m128d result = _mm_addsub_pd(a, b);
|
|
result = _mm_movedup_pd(result);
|
|
return 0;
|
|
}"
|
|
SSE3_FOUND)
|
|
|
|
# Check AVX
|
|
set(CMAKE_REQUIRED_FLAGS ${AVX_FLAG})
|
|
set(AVX_FOUND_EXITCODE
|
|
1
|
|
CACHE STRING "Result from TRY_RUN" FORCE)
|
|
check_cxx_source_runs(
|
|
"
|
|
#include <immintrin.h>
|
|
int main()
|
|
{
|
|
__m256 a = _mm256_set_ps(-1.0f, 2.0f, -3.0f, 4.0f, -1.0f, 2.0f, -3.0f, 4.0f);
|
|
__m256 b = _mm256_set_ps(1.0f, 2.0f, 3.0f, 4.0f, 1.0f, 2.0f, 3.0f, 4.0f);
|
|
__m256 result = _mm256_add_ps(a, b);
|
|
return 0;
|
|
}"
|
|
AVX_FOUND)
|
|
|
|
# Check AVX 2
|
|
set(CMAKE_REQUIRED_FLAGS ${AVX2_FLAG})
|
|
set(AVX2_FOUND_EXITCODE
|
|
1
|
|
CACHE STRING "Result from TRY_RUN" FORCE)
|
|
check_cxx_source_runs(
|
|
"
|
|
#include <immintrin.h>
|
|
int main()
|
|
{
|
|
__m256i a = _mm256_set_epi32 (-1, 2, -3, 4, -1, 2, -3, 4);
|
|
__m256i result = _mm256_abs_epi32 (a);
|
|
return 0;
|
|
}"
|
|
AVX2_FOUND)
|
|
|
|
# Check AVX512F
|
|
set(CMAKE_REQUIRED_FLAGS ${AVX512F_FLAG})
|
|
set(AVX512F_FOUND_EXITCODE
|
|
1
|
|
CACHE STRING "Result from TRY_RUN" FORCE)
|
|
check_cxx_source_runs(
|
|
"
|
|
#include <immintrin.h>
|
|
int main()
|
|
{
|
|
__m512i a = _mm512_set_epi32 (-1, 2, -3, 4, -1, 2, -3, 4,
|
|
13, -5, 6, -7, 9, 2, -6, 3);
|
|
__m512i result = _mm512_abs_epi32 (a);
|
|
return 0;
|
|
}"
|
|
AVX512F_FOUND)
|
|
if(AVX512F_FOUND)
|
|
add_definitions(-DPADDLE_WITH_AVX512F)
|
|
endif()
|
|
|
|
set(CMAKE_REQUIRED_FLAGS ${CMAKE_REQUIRED_FLAGS_RETAINED})
|
|
mark_as_advanced(MMX_FOUND SSE2_FOUND SSE3_FOUND AVX_FOUND AVX2_FOUND
|
|
AVX512F_FOUND)
|