forked from apache/orc
-
Notifications
You must be signed in to change notification settings - Fork 0
/
ConfigSimdLevel.cmake
104 lines (94 loc) · 3.83 KB
/
ConfigSimdLevel.cmake
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
# Licensed to the Apache Software Foundation (ASF) under one
# or more contributor license agreements. See the NOTICE file
# distributed with this work for additional information
# regarding copyright ownership. The ASF licenses this file
# to you under the Apache License, Version 2.0 (the
# "License"); you may not use this file except in compliance
# with the License. You may obtain a copy of the License at
#
# http://www.apache.org/licenses/LICENSE-2.0
#
# Unless required by applicable law or agreed to in writing,
# software distributed under the License is distributed on an
# "AS IS" BASIS, WITHOUT WARRANTIES OR CONDITIONS OF ANY
# KIND, either express or implied. See the License for the
# specific language governing permissions and limitations
# under the License.
INCLUDE(CheckCXXSourceRuns)
INCLUDE(CheckCXXCompilerFlag)
message(STATUS "System processor: ${CMAKE_SYSTEM_PROCESSOR}")
if(NOT DEFINED ORC_SIMD_LEVEL)
set(ORC_SIMD_LEVEL
"DEFAULT"
CACHE STRING "Compile time SIMD optimization level")
endif()
if(NOT DEFINED ORC_CPU_FLAG)
if(CMAKE_SYSTEM_PROCESSOR MATCHES "AMD64|X86|x86|i[3456]86|x64")
set(ORC_CPU_FLAG "x86")
else()
message(STATUS "Unsupported system processor for SIMD optimization")
endif()
endif()
# Check architecture specific compiler flags
if(ORC_CPU_FLAG STREQUAL "x86")
# x86/amd64 compiler flags, msvc/gcc/clang
if(MSVC)
set(ORC_AVX512_FLAG "/arch:AVX512")
check_cxx_compiler_flag(${ORC_AVX512_FLAG} COMPILER_SUPPORT_AVX512)
else()
# "arch=native" selects the CPU to generate code for at compilation time by determining the processor type of the compiling machine.
# Using -march=native enables all instruction subsets supported by the local machine.
# Using -mtune=native produces code optimized for the local machine under the constraints of the selected instruction set.
set(ORC_AVX512_FLAG "-march=native -mtune=native")
check_cxx_compiler_flag("-mavx512f -mavx512cd -mavx512vl -mavx512dq -mavx512bw" COMPILER_SUPPORT_AVX512)
endif()
if(MINGW)
# https://gcc.gnu.org/bugzilla/show_bug.cgi?id=65782
message(STATUS "Disable AVX512 support on MINGW for now")
else()
# Check for AVX512 support in the compiler.
set(OLD_CMAKE_REQURED_FLAGS ${CMAKE_REQUIRED_FLAGS})
set(CMAKE_REQUIRED_FLAGS "${CMAKE_REQUIRED_FLAGS} ${ORC_AVX512_FLAG}")
CHECK_CXX_SOURCE_COMPILES("
#ifdef _MSC_VER
#include <intrin.h>
#else
#include <immintrin.h>
#endif
int main() {
__m512i mask = _mm512_set1_epi32(0x1);
char out[32];
_mm512_storeu_si512(out, mask);
return 0;
}"
CXX_SUPPORTS_AVX512)
set(CMAKE_REQUIRED_FLAGS ${OLD_CMAKE_REQURED_FLAGS})
endif()
if(CXX_SUPPORTS_AVX512)
execute_process(COMMAND grep flags /proc/cpuinfo
COMMAND head -1
OUTPUT_VARIABLE flags_ver)
message(STATUS "CPU ${flags_ver}")
execute_process(COMMAND grep avx512f /proc/cpuinfo
COMMAND head -1
OUTPUT_VARIABLE CPU_HAS_AVX512)
endif()
# Runtime SIMD level it can get from compiler
if(CPU_HAS_AVX512 AND CXX_SUPPORTS_AVX512 AND COMPILER_SUPPORT_AVX512)
message(STATUS "Enabled the AVX512 for RLE bit-unpacking")
set(ORC_SIMD_LEVEL "AVX512")
add_definitions(-DORC_HAVE_RUNTIME_AVX512)
else()
message(STATUS "WARNING: AVX512 required but compiler doesn't support it, failed to enable AVX512.")
set(BUILD_ENABLE_AVX512 OFF)
endif()
if(ORC_SIMD_LEVEL STREQUAL "DEFAULT")
set(ORC_SIMD_LEVEL "NONE")
endif()
if(ORC_SIMD_LEVEL STREQUAL "AVX512")
set(CMAKE_CXX_FLAGS "${CMAKE_CXX_FLAGS} ${ORC_AVX512_FLAG}")
message(STATUS "ORC_HAVE_RUNTIME_AVX512 defined, ORC_SIMD_LEVEL: ${ORC_SIMD_LEVEL}")
else()
message(STATUS "ORC_HAVE_RUNTIME_AVX512 not defined, ORC_SIMD_LEVEL: ${ORC_SIMD_LEVEL}")
endif()
endif()