mirror of
https://github.com/tesseract-ocr/tesseract.git
synced 2024-11-24 02:59:07 +08:00
cmake: add detection of AVX, AVX2, SSE41
This commit is contained in:
parent
29ab1a42cc
commit
b9f7bb2b89
@ -175,6 +175,38 @@ endif()
|
||||
#
|
||||
###############################################################################
|
||||
|
||||
# auto optimize
|
||||
include(OptimizeForArchitecture)
|
||||
AutodetectHostArchitecture()
|
||||
OptimizeForArchitecture()
|
||||
foreach(flag ${Vc_ARCHITECTURE_FLAGS})
|
||||
set(CMAKE_CXX_FLAGS "${CMAKE_CXX_FLAGS} ${flag}")
|
||||
endforeach()
|
||||
|
||||
# add definition as expected in src/arch/simddetect.cpp
|
||||
set(AVX_OPT 0)
|
||||
set(AVX2_OPT 0)
|
||||
set(SSE41_OPT 0)
|
||||
set(MARCH_NATIVE_OPT 0)
|
||||
foreach(flag ${_enable_vector_unit_list}) # from OptimizeForArchitecture()
|
||||
string(TOUPPER "${flag}" flag)
|
||||
string(REPLACE "\." "_" flag "${flag}")
|
||||
set(sim_flags "${sim_flags} -D${flag}")
|
||||
string(REPLACE "_" "" flag "${flag}")
|
||||
if("${flag}" MATCHES "AVX|AVX2|SSE41")
|
||||
set("${flag}_OPT" 1)
|
||||
endif()
|
||||
endforeach(flag)
|
||||
FILE(GLOB arch_files "src/arch/*.cpp")
|
||||
set_source_files_properties(${arch_files} PROPERTIES COMPILE_FLAGS "${CMAKE_CXX_FLAGS} ${sim_flags}")
|
||||
include(CheckCXXCompilerFlag)
|
||||
CHECK_CXX_COMPILER_FLAG("-march=native" COMPILER_SUPPORTS_MARCH_NATIVE)
|
||||
if(COMPILER_SUPPORTS_MARCH_NATIVE)
|
||||
set(CMAKE_CXX_FLAGS "${CMAKE_CXX_FLAGS} -march=native -mtune=native")
|
||||
set_source_files_properties(src/arch/dotproduct.cpp PROPERTIES COMPILE_FLAGS "${CMAKE_CXX_FLAGS} -O3 -ffast-math")
|
||||
set(MARCH_NATIVE_OPT 1)
|
||||
endif()
|
||||
|
||||
set(AUTOCONFIG_SRC ${CMAKE_CURRENT_BINARY_DIR}/config_auto.h.in)
|
||||
set(AUTOCONFIG ${CMAKE_CURRENT_BINARY_DIR}/config_auto.h)
|
||||
add_definitions(-DHAVE_CONFIG_H)
|
||||
@ -243,7 +275,9 @@ endif()
|
||||
########################################
|
||||
|
||||
file(GLOB tesseract_src
|
||||
src/arch/*.cpp
|
||||
src/arch/simddetect.cpp
|
||||
src/arch/intsimdmatrix.cpp
|
||||
src/arch/dotproduct.cpp
|
||||
src/ccmain/*.cpp
|
||||
src/ccstruct/*.cpp
|
||||
src/ccutil/*.cpp
|
||||
@ -256,6 +290,17 @@ file(GLOB tesseract_src
|
||||
src/viewer/*.cpp
|
||||
src/wordrec/*.cpp
|
||||
)
|
||||
|
||||
if(AVX_OPT)
|
||||
list(APPEND tesseract_src src/arch/dotproductavx.cpp)
|
||||
endif(AVX_OPT)
|
||||
if(AVX2_OPT)
|
||||
list(APPEND tesseract_src src/arch/intsimdmatrixavx2.cpp)
|
||||
endif(AVX2_OPT)
|
||||
if(SSE41_OPT)
|
||||
list(APPEND tesseract_src src/arch/dotproductsse.cpp src/arch/intsimdmatrixsse.cpp)
|
||||
endif(SSE41_OPT)
|
||||
|
||||
file(GLOB tesseract_hdr
|
||||
src/api/*.h
|
||||
src/arch/*.h
|
||||
@ -290,56 +335,7 @@ if (WIN32)
|
||||
${tesseract_hdr}
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/vs2010/tesseract/resource.h)
|
||||
set(tesseract_rsc ${CMAKE_CURRENT_BINARY_DIR}/vs2010/tesseract/libtesseract.rc)
|
||||
if (NOT CLANG)
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/dotproductsse.cpp
|
||||
PROPERTIES COMPILE_DEFINITIONS __SSE4_1__)
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/intsimdmatrixsse.cpp
|
||||
PROPERTIES COMPILE_DEFINITIONS __SSE4_1__)
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/dotproductavx.cpp
|
||||
PROPERTIES COMPILE_FLAGS "/arch:AVX")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/intsimdmatrixavx2.cpp
|
||||
PROPERTIES COMPILE_FLAGS "/arch:AVX2")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/simddetect.cpp
|
||||
PROPERTIES COMPILE_FLAGS "/DAVX /DAVX2 /DSSE4_1")
|
||||
else(CLANG)
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/dotproductsse.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-msse4.1")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/intsimdmatrixsse.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-msse4.1")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/dotproductavx.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-mavx")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/intsimdmatrixavx2.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-mavx2")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/simddetect.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-DAVX -DAVX2 -DSSE4_1")
|
||||
endif() # NOT CLANG
|
||||
endif() # MSVC
|
||||
else()
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/dotproductsse.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-msse4.1")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/intsimdmatrixsse.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-msse4.1")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/dotproductavx.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-mavx")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/intsimdmatrixavx2.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-mavx2")
|
||||
set_source_files_properties(
|
||||
${CMAKE_CURRENT_SOURCE_DIR}/src/arch/simddetect.cpp
|
||||
PROPERTIES COMPILE_FLAGS "-DAVX -DAVX2 -DSSE4_1")
|
||||
endif()
|
||||
|
||||
add_library (libtesseract ${LIBRARY_TYPE} ${tesseract_src} ${tesseract_hdr}
|
||||
|
130
cmake/AddCompilerFlag.cmake
Normal file
130
cmake/AddCompilerFlag.cmake
Normal file
@ -0,0 +1,130 @@
|
||||
# - Add a given compiler flag to flags variables.
|
||||
# AddCompilerFlag(<flag> [<var>])
|
||||
# or
|
||||
# AddCompilerFlag(<flag> [C_FLAGS <var>] [CXX_FLAGS <var>] [C_RESULT <var>]
|
||||
# [CXX_RESULT <var>])
|
||||
|
||||
#=============================================================================
|
||||
# Copyright 2010-2015 Matthias Kretz <kretz@kde.org>
|
||||
#
|
||||
# Redistribution and use in source and binary forms, with or without
|
||||
# modification, are permitted provided that the following conditions are
|
||||
# met:
|
||||
#
|
||||
# * Redistributions of source code must retain the above copyright notice,
|
||||
# this list of conditions and the following disclaimer.
|
||||
#
|
||||
# * Redistributions in binary form must reproduce the above copyright notice,
|
||||
# this list of conditions and the following disclaimer in the documentation
|
||||
# and/or other materials provided with the distribution.
|
||||
#
|
||||
# * Neither the names of contributing organizations nor the
|
||||
# names of its contributors may be used to endorse or promote products
|
||||
# derived from this software without specific prior written permission.
|
||||
#
|
||||
# THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDER AND CONTRIBUTORS ``AS IS''
|
||||
# AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT LIMITED TO, THE
|
||||
# IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR A PARTICULAR PURPOSE
|
||||
# ARE DISCLAIMED. IN NO EVENT SHALL THE AUTHORS OR CONTRIBUTORS BE LIABLE FOR
|
||||
# ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL, EXEMPLARY, OR CONSEQUENTIAL
|
||||
# DAMAGES (INCLUDING, BUT NOT LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR
|
||||
# SERVICES; LOSS OF USE, DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER
|
||||
# CAUSED AND ON ANY THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY,
|
||||
# OR TORT (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE
|
||||
# OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
|
||||
#=============================================================================
|
||||
|
||||
get_filename_component(_currentDir "${CMAKE_CURRENT_LIST_FILE}" PATH)
|
||||
include("${_currentDir}/CheckCCompilerFlag.cmake")
|
||||
include("${_currentDir}/CheckCXXCompilerFlag.cmake")
|
||||
|
||||
macro(AddCompilerFlag _flag)
|
||||
string(REGEX REPLACE "[-.+/:= ]" "_" _flag_esc "${_flag}")
|
||||
|
||||
set(_c_flags "CMAKE_C_FLAGS")
|
||||
set(_cxx_flags "CMAKE_CXX_FLAGS")
|
||||
set(_c_result tmp)
|
||||
set(_cxx_result tmp)
|
||||
if(${ARGC} EQUAL 2)
|
||||
message(WARNING "Deprecated use of the AddCompilerFlag macro.")
|
||||
unset(_c_result)
|
||||
set(_cxx_result ${ARGV1})
|
||||
elseif(${ARGC} GREATER 2)
|
||||
set(state 0)
|
||||
unset(_c_flags)
|
||||
unset(_cxx_flags)
|
||||
unset(_c_result)
|
||||
unset(_cxx_result)
|
||||
foreach(_arg ${ARGN})
|
||||
if("x${_arg}" STREQUAL "xC_FLAGS")
|
||||
set(state 1)
|
||||
if(NOT DEFINED _c_result)
|
||||
set(_c_result tmp0)
|
||||
endif()
|
||||
elseif("x${_arg}" STREQUAL "xCXX_FLAGS")
|
||||
set(state 2)
|
||||
if(NOT DEFINED _cxx_result)
|
||||
set(_cxx_result tmp1)
|
||||
endif()
|
||||
elseif("x${_arg}" STREQUAL "xC_RESULT")
|
||||
set(state 3)
|
||||
elseif("x${_arg}" STREQUAL "xCXX_RESULT")
|
||||
set(state 4)
|
||||
elseif(state EQUAL 1)
|
||||
set(_c_flags "${_arg}")
|
||||
elseif(state EQUAL 2)
|
||||
set(_cxx_flags "${_arg}")
|
||||
elseif(state EQUAL 3)
|
||||
set(_c_result "${_arg}")
|
||||
elseif(state EQUAL 4)
|
||||
set(_cxx_result "${_arg}")
|
||||
else()
|
||||
message(FATAL_ERROR "Syntax error for AddCompilerFlag")
|
||||
endif()
|
||||
endforeach()
|
||||
endif()
|
||||
|
||||
set(_c_code "int main() { return 0; }")
|
||||
set(_cxx_code "int main() { return 0; }")
|
||||
if("${_flag}" STREQUAL "-mfma")
|
||||
# Compiling with FMA3 support may fail only at the assembler level.
|
||||
# In that case we need to have such an instruction in the test code
|
||||
set(_c_code "#include <immintrin.h>
|
||||
__m128 foo(__m128 x) { return _mm_fmadd_ps(x, x, x); }
|
||||
int main() { return 0; }")
|
||||
set(_cxx_code "${_c_code}")
|
||||
elseif("${_flag}" STREQUAL "-stdlib=libc++")
|
||||
# Compiling with libc++ not only requires a compiler that understands it, but also
|
||||
# the libc++ headers itself
|
||||
set(_cxx_code "#include <iostream>
|
||||
#include <cstdio>
|
||||
int main() { return 0; }")
|
||||
else()
|
||||
set(_cxx_code "#include <cstdio>
|
||||
int main() { return 0; }")
|
||||
endif()
|
||||
|
||||
if(DEFINED _c_result)
|
||||
check_c_compiler_flag("${_flag}" check_c_compiler_flag_${_flag_esc} "${_c_code}")
|
||||
set(${_c_result} ${check_c_compiler_flag_${_flag_esc}})
|
||||
endif()
|
||||
if(DEFINED _cxx_result)
|
||||
check_cxx_compiler_flag("${_flag}" check_cxx_compiler_flag_${_flag_esc} "${_cxx_code}")
|
||||
set(${_cxx_result} ${check_cxx_compiler_flag_${_flag_esc}})
|
||||
endif()
|
||||
|
||||
macro(my_append _list _flag _special)
|
||||
if("x${_list}" STREQUAL "x${_special}")
|
||||
set(${_list} "${${_list}} ${_flag}")
|
||||
else()
|
||||
list(APPEND ${_list} "${_flag}")
|
||||
endif()
|
||||
endmacro()
|
||||
|
||||
if(check_c_compiler_flag_${_flag_esc} AND DEFINED _c_flags)
|
||||
my_append(${_c_flags} "${_flag}" CMAKE_C_FLAGS)
|
||||
endif()
|
||||
if(check_cxx_compiler_flag_${_flag_esc} AND DEFINED _cxx_flags)
|
||||
my_append(${_cxx_flags} "${_flag}" CMAKE_CXX_FLAGS)
|
||||
endif()
|
||||
endmacro(AddCompilerFlag)
|
73
cmake/CheckCCompilerFlag.cmake
Normal file
73
cmake/CheckCCompilerFlag.cmake
Normal file
@ -0,0 +1,73 @@
|
||||
# - Check whether the C compiler supports a given flag.
|
||||
# CHECK_C_COMPILER_FLAG(<flag> <var>)
|
||||
# <flag> - the compiler flag
|
||||
# <var> - variable to store the result
|
||||
# This internally calls the check_c_source_compiles macro.
|
||||
# See help for CheckCSourceCompiles for a listing of variables
|
||||
# that can modify the build.
|
||||
|
||||
#=============================================================================
|
||||
# Copyright 2006-2009 Kitware, Inc.
|
||||
# Copyright 2006 Alexander Neundorf <neundorf@kde.org>
|
||||
# Copyright 2011-2013 Matthias Kretz <kretz@kde.org>
|
||||
#
|
||||
# Redistribution and use in source and binary forms, with or without
|
||||
# modification, are permitted provided that the following conditions are
|
||||
# met:
|
||||
#
|
||||
# * Redistributions of source code must retain the above copyright notice,
|
||||
# this list of conditions and the following disclaimer.
|
||||
#
|
||||
# * Redistributions in binary form must reproduce the above copyright notice,
|
||||
# this list of conditions and the following disclaimer in the documentation
|
||||
# and/or other materials provided with the distribution.
|
||||
#
|
||||
# * The names of Kitware, Inc., the Insight Consortium, or the names of
|
||||
# any consortium members, or of any contributors, may not be used to
|
||||
# endorse or promote products derived from this software without
|
||||
# specific prior written permission.
|
||||
#
|
||||
# THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDER AND CONTRIBUTORS ``AS IS''
|
||||
# AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT LIMITED TO, THE
|
||||
# IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR A PARTICULAR PURPOSE
|
||||
# ARE DISCLAIMED. IN NO EVENT SHALL THE AUTHORS OR CONTRIBUTORS BE LIABLE FOR
|
||||
# ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL, EXEMPLARY, OR CONSEQUENTIAL
|
||||
# DAMAGES (INCLUDING, BUT NOT LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR
|
||||
# SERVICES; LOSS OF USE, DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER
|
||||
# CAUSED AND ON ANY THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY,
|
||||
# OR TORT (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE
|
||||
# OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
|
||||
#=============================================================================
|
||||
|
||||
INCLUDE(CheckCSourceCompiles)
|
||||
|
||||
MACRO (CHECK_C_COMPILER_FLAG _FLAG _RESULT)
|
||||
SET(SAFE_CMAKE_REQUIRED_DEFINITIONS "${CMAKE_REQUIRED_DEFINITIONS}")
|
||||
SET(CMAKE_REQUIRED_DEFINITIONS "${_FLAG}")
|
||||
if(${ARGC} GREATER 2)
|
||||
SET(TEST_SOURCE "${ARGV2}")
|
||||
else()
|
||||
SET(TEST_SOURCE "int main() { return 0;}")
|
||||
endif()
|
||||
CHECK_C_SOURCE_COMPILES("${TEST_SOURCE}" ${_RESULT}
|
||||
# Some compilers do not fail with a bad flag
|
||||
FAIL_REGEX "error: bad value (.*) for .* switch" # GNU
|
||||
FAIL_REGEX "argument unused during compilation" # clang
|
||||
FAIL_REGEX "is valid for .* but not for C" # GNU
|
||||
FAIL_REGEX "unrecognized .*option" # GNU
|
||||
FAIL_REGEX "ignored for target" # GNU
|
||||
FAIL_REGEX "ignoring unknown option" # MSVC
|
||||
FAIL_REGEX "warning D9002" # MSVC
|
||||
FAIL_REGEX "[Uu]nknown option" # HP
|
||||
FAIL_REGEX "[Ww]arning: [Oo]ption" # SunPro
|
||||
FAIL_REGEX "command option .* is not recognized" # XL
|
||||
FAIL_REGEX "WARNING: unknown flag:" # Open64
|
||||
FAIL_REGEX "command line error" # ICC
|
||||
FAIL_REGEX "command line warning" # ICC
|
||||
FAIL_REGEX "#10236:" # ICC: File not found
|
||||
FAIL_REGEX " #10159: " # ICC
|
||||
FAIL_REGEX " #10353: " # ICC: option '-mfma' ignored, suggest using '-march=core-avx2'
|
||||
)
|
||||
SET (CMAKE_REQUIRED_DEFINITIONS "${SAFE_CMAKE_REQUIRED_DEFINITIONS}")
|
||||
ENDMACRO (CHECK_C_COMPILER_FLAG)
|
||||
|
73
cmake/CheckCXXCompilerFlag.cmake
Normal file
73
cmake/CheckCXXCompilerFlag.cmake
Normal file
@ -0,0 +1,73 @@
|
||||
# - Check whether the CXX compiler supports a given flag.
|
||||
# CHECK_CXX_COMPILER_FLAG(<flag> <var>)
|
||||
# <flag> - the compiler flag
|
||||
# <var> - variable to store the result
|
||||
# This internally calls the check_cxx_source_compiles macro. See help
|
||||
# for CheckCXXSourceCompiles for a listing of variables that can
|
||||
# modify the build.
|
||||
|
||||
#=============================================================================
|
||||
# Copyright 2006-2009 Kitware, Inc.
|
||||
# Copyright 2006 Alexander Neundorf <neundorf@kde.org>
|
||||
# Copyright 2011-2013 Matthias Kretz <kretz@kde.org>
|
||||
#
|
||||
# Redistribution and use in source and binary forms, with or without
|
||||
# modification, are permitted provided that the following conditions are
|
||||
# met:
|
||||
#
|
||||
# * Redistributions of source code must retain the above copyright notice,
|
||||
# this list of conditions and the following disclaimer.
|
||||
#
|
||||
# * Redistributions in binary form must reproduce the above copyright notice,
|
||||
# this list of conditions and the following disclaimer in the documentation
|
||||
# and/or other materials provided with the distribution.
|
||||
#
|
||||
# * The names of Kitware, Inc., the Insight Consortium, or the names of
|
||||
# any consortium members, or of any contributors, may not be used to
|
||||
# endorse or promote products derived from this software without
|
||||
# specific prior written permission.
|
||||
#
|
||||
# THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDER AND CONTRIBUTORS ``AS IS''
|
||||
# AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT LIMITED TO, THE
|
||||
# IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR A PARTICULAR PURPOSE
|
||||
# ARE DISCLAIMED. IN NO EVENT SHALL THE AUTHORS OR CONTRIBUTORS BE LIABLE FOR
|
||||
# ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL, EXEMPLARY, OR CONSEQUENTIAL
|
||||
# DAMAGES (INCLUDING, BUT NOT LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR
|
||||
# SERVICES; LOSS OF USE, DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER
|
||||
# CAUSED AND ON ANY THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY,
|
||||
# OR TORT (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE
|
||||
# OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
|
||||
#=============================================================================
|
||||
|
||||
INCLUDE(CheckCXXSourceCompiles)
|
||||
|
||||
MACRO (CHECK_CXX_COMPILER_FLAG _FLAG _RESULT)
|
||||
SET(SAFE_CMAKE_REQUIRED_DEFINITIONS "${CMAKE_REQUIRED_DEFINITIONS}")
|
||||
SET(CMAKE_REQUIRED_DEFINITIONS "${_FLAG}")
|
||||
if(${ARGC} GREATER 2)
|
||||
SET(TEST_SOURCE "${ARGV2}")
|
||||
else()
|
||||
SET(TEST_SOURCE "int main() { return 0;}")
|
||||
endif()
|
||||
CHECK_CXX_SOURCE_COMPILES("${TEST_SOURCE}" ${_RESULT}
|
||||
# Some compilers do not fail with a bad flag
|
||||
FAIL_REGEX "error: bad value (.*) for .* switch" # GNU
|
||||
FAIL_REGEX "argument unused during compilation" # clang
|
||||
FAIL_REGEX "is valid for .* but not for C\\\\+\\\\+" # GNU
|
||||
FAIL_REGEX "unrecognized .*option" # GNU
|
||||
FAIL_REGEX "ignored for target" # GNU
|
||||
FAIL_REGEX "ignoring unknown option" # MSVC
|
||||
FAIL_REGEX "warning D9002" # MSVC
|
||||
FAIL_REGEX "[Uu]nknown option" # HP
|
||||
FAIL_REGEX "[Ww]arning: [Oo]ption" # SunPro
|
||||
FAIL_REGEX "command option .* is not recognized" # XL
|
||||
FAIL_REGEX "WARNING: unknown flag:" # Open64
|
||||
FAIL_REGEX "command line error" # ICC
|
||||
FAIL_REGEX "command line warning" # ICC
|
||||
FAIL_REGEX "#10236:" # ICC: File not found
|
||||
FAIL_REGEX " #10159: " # ICC
|
||||
FAIL_REGEX " #10353: " # ICC: option '-mfma' ignored, suggest using '-march=core-avx2'
|
||||
)
|
||||
SET (CMAKE_REQUIRED_DEFINITIONS "${SAFE_CMAKE_REQUIRED_DEFINITIONS}")
|
||||
ENDMACRO (CHECK_CXX_COMPILER_FLAG)
|
||||
|
581
cmake/OptimizeForArchitecture.cmake
Normal file
581
cmake/OptimizeForArchitecture.cmake
Normal file
@ -0,0 +1,581 @@
|
||||
# Determine the host CPU feature set and determine the best set of compiler
|
||||
# flags to enable all supported SIMD relevant features. Alternatively, the
|
||||
# target CPU can be explicitly selected (for generating more generic binaries
|
||||
# or for targeting a different system).
|
||||
# Compilers provide e.g. the -march=native flag to achieve a similar result.
|
||||
# This fails to address the need for building for a different microarchitecture
|
||||
# than the current host.
|
||||
# The script tries to deduce all settings from the model and family numbers of
|
||||
# the CPU instead of reading the CPUID flags from e.g. /proc/cpuinfo. This makes
|
||||
# the detection more independent from the CPUID code in the kernel (e.g. avx2 is
|
||||
# not listed on older kernels).
|
||||
#
|
||||
# Usage:
|
||||
# OptimizeForArchitecture()
|
||||
# If either of Vc_SSE_INTRINSICS_BROKEN, Vc_AVX_INTRINSICS_BROKEN,
|
||||
# Vc_AVX2_INTRINSICS_BROKEN is defined and set, the OptimizeForArchitecture
|
||||
# macro will consequently disable the relevant features via compiler flags.
|
||||
|
||||
#=============================================================================
|
||||
# Copyright 2010-2016 Matthias Kretz <kretz@kde.org>
|
||||
#
|
||||
# Redistribution and use in source and binary forms, with or without
|
||||
# modification, are permitted provided that the following conditions are
|
||||
# met:
|
||||
#
|
||||
# * Redistributions of source code must retain the above copyright notice,
|
||||
# this list of conditions and the following disclaimer.
|
||||
# * Redistributions in binary form must reproduce the above copyright notice,
|
||||
# this list of conditions and the following disclaimer in the documentation
|
||||
# and/or other materials provided with the distribution.
|
||||
# * Neither the names of contributing organizations nor the
|
||||
# names of its contributors may be used to endorse or promote products
|
||||
# derived from this software without specific prior written permission.
|
||||
#
|
||||
# THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDER AND CONTRIBUTORS ``AS IS''
|
||||
# AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT LIMITED TO, THE
|
||||
# IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR A PARTICULAR PURPOSE
|
||||
# ARE DISCLAIMED. IN NO EVENT SHALL THE AUTHORS OR CONTRIBUTORS BE LIABLE FOR
|
||||
# ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL, EXEMPLARY, OR CONSEQUENTIAL
|
||||
# DAMAGES (INCLUDING, BUT NOT LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR
|
||||
# SERVICES; LOSS OF USE, DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER
|
||||
# CAUSED AND ON ANY THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY,
|
||||
# OR TORT (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE
|
||||
# OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
|
||||
#=============================================================================
|
||||
|
||||
get_filename_component(_currentDir "${CMAKE_CURRENT_LIST_FILE}" PATH)
|
||||
include("${_currentDir}/AddCompilerFlag.cmake")
|
||||
include(CheckIncludeFileCXX)
|
||||
|
||||
macro(_my_find _list _value _ret)
|
||||
list(FIND ${_list} "${_value}" _found)
|
||||
if(_found EQUAL -1)
|
||||
set(${_ret} FALSE)
|
||||
else(_found EQUAL -1)
|
||||
set(${_ret} TRUE)
|
||||
endif(_found EQUAL -1)
|
||||
endmacro(_my_find)
|
||||
|
||||
macro(AutodetectHostArchitecture)
|
||||
set(TARGET_ARCHITECTURE "generic")
|
||||
set(Vc_ARCHITECTURE_FLAGS)
|
||||
set(_vendor_id)
|
||||
set(_cpu_family)
|
||||
set(_cpu_model)
|
||||
if(CMAKE_SYSTEM_NAME STREQUAL "Linux")
|
||||
file(READ "/proc/cpuinfo" _cpuinfo)
|
||||
string(REGEX REPLACE ".*vendor_id[ \t]*:[ \t]+([a-zA-Z0-9_-]+).*" "\\1" _vendor_id "${_cpuinfo}")
|
||||
string(REGEX REPLACE ".*cpu family[ \t]*:[ \t]+([a-zA-Z0-9_-]+).*" "\\1" _cpu_family "${_cpuinfo}")
|
||||
string(REGEX REPLACE ".*model[ \t]*:[ \t]+([a-zA-Z0-9_-]+).*" "\\1" _cpu_model "${_cpuinfo}")
|
||||
string(REGEX REPLACE ".*flags[ \t]*:[ \t]+([^\n]+).*" "\\1" _cpu_flags "${_cpuinfo}")
|
||||
elseif(CMAKE_SYSTEM_NAME STREQUAL "Darwin")
|
||||
exec_program("/usr/sbin/sysctl -n machdep.cpu.vendor machdep.cpu.model machdep.cpu.family machdep.cpu.features" OUTPUT_VARIABLE _sysctl_output_string)
|
||||
string(REPLACE "\n" ";" _sysctl_output ${_sysctl_output_string})
|
||||
list(GET _sysctl_output 0 _vendor_id)
|
||||
list(GET _sysctl_output 1 _cpu_model)
|
||||
list(GET _sysctl_output 2 _cpu_family)
|
||||
list(GET _sysctl_output 3 _cpu_flags)
|
||||
|
||||
string(TOLOWER "${_cpu_flags}" _cpu_flags)
|
||||
string(REPLACE "." "_" _cpu_flags "${_cpu_flags}")
|
||||
elseif(CMAKE_SYSTEM_NAME STREQUAL "Windows")
|
||||
get_filename_component(_vendor_id "[HKEY_LOCAL_MACHINE\\Hardware\\Description\\System\\CentralProcessor\\0;VendorIdentifier]" NAME CACHE)
|
||||
get_filename_component(_cpu_id "[HKEY_LOCAL_MACHINE\\Hardware\\Description\\System\\CentralProcessor\\0;Identifier]" NAME CACHE)
|
||||
mark_as_advanced(_vendor_id _cpu_id)
|
||||
string(REGEX REPLACE ".* Family ([0-9]+) .*" "\\1" _cpu_family "${_cpu_id}")
|
||||
string(REGEX REPLACE ".* Model ([0-9]+) .*" "\\1" _cpu_model "${_cpu_id}")
|
||||
endif(CMAKE_SYSTEM_NAME STREQUAL "Linux")
|
||||
if(_vendor_id STREQUAL "GenuineIntel")
|
||||
if(_cpu_family EQUAL 6)
|
||||
# taken from the Intel ORM
|
||||
# http://www.intel.com/content/www/us/en/processors/architectures-software-developer-manuals.html
|
||||
# CPUID Signature Values of Of Recent Intel Microarchitectures
|
||||
# 4E 5E | Skylake microarchitecture
|
||||
# 3D 47 56 | Broadwell microarchitecture
|
||||
# 3C 45 46 3F | Haswell microarchitecture
|
||||
# 3A 3E | Ivy Bridge microarchitecture
|
||||
# 2A 2D | Sandy Bridge microarchitecture
|
||||
# 25 2C 2F | Intel microarchitecture Westmere
|
||||
# 1A 1E 1F 2E | Intel microarchitecture Nehalem
|
||||
# 17 1D | Enhanced Intel Core microarchitecture
|
||||
# 0F | Intel Core microarchitecture
|
||||
#
|
||||
# Intel SDM Vol. 3C 35-1 / December 2016:
|
||||
# 57 | Xeon Phi 3200, 5200, 7200 [Knights Landing]
|
||||
# 85 | Future Xeon Phi
|
||||
# 8E 9E | 7th gen. Core [Kaby Lake]
|
||||
# 55 | Future Xeon [Skylake w/ AVX512]
|
||||
# 4E 5E | 6th gen. Core / E3 v5 [Skylake w/o AVX512]
|
||||
# 56 | Xeon D-1500 [Broadwell]
|
||||
# 4F | Xeon E5 v4, E7 v4, i7-69xx [Broadwell]
|
||||
# 47 | 5th gen. Core / Xeon E3 v4 [Broadwell]
|
||||
# 3D | M-5xxx / 5th gen. [Broadwell]
|
||||
# 3F | Xeon E5 v3, E7 v3, i7-59xx [Haswell-E]
|
||||
# 3C 45 46 | 4th gen. Core, Xeon E3 v3 [Haswell]
|
||||
# 3E | Xeon E5 v2, E7 v2, i7-49xx [Ivy Bridge-E]
|
||||
# 3A | 3rd gen. Core, Xeon E3 v2 [Ivy Bridge]
|
||||
# 2D | Xeon E5, i7-39xx [Sandy Bridge]
|
||||
# 2F | Xeon E7
|
||||
# 2A | Xeon E3, 2nd gen. Core [Sandy Bridge]
|
||||
# 2E | Xeon 7500, 6500 series
|
||||
# 25 2C | Xeon 3600, 5600 series, Core i7, i5 and i3
|
||||
#
|
||||
# Values from the Intel SDE:
|
||||
# 5C | Goldmont
|
||||
# 5A | Silvermont
|
||||
# 57 | Knights Landing
|
||||
# 66 | Cannonlake
|
||||
# 55 | Skylake Server
|
||||
# 4E | Skylake Client
|
||||
# 3C | Broadwell (likely a bug in the SDE)
|
||||
# 3C | Haswell
|
||||
if(_cpu_model EQUAL 87) # 57
|
||||
set(TARGET_ARCHITECTURE "knl") # Knights Landing
|
||||
elseif(_cpu_model EQUAL 92)
|
||||
set(TARGET_ARCHITECTURE "goldmont")
|
||||
elseif(_cpu_model EQUAL 90 OR _cpu_model EQUAL 76)
|
||||
set(TARGET_ARCHITECTURE "silvermont")
|
||||
elseif(_cpu_model EQUAL 102)
|
||||
set(TARGET_ARCHITECTURE "cannonlake")
|
||||
elseif(_cpu_model EQUAL 142 OR _cpu_model EQUAL 158) # 8E, 9E
|
||||
set(TARGET_ARCHITECTURE "kaby-lake")
|
||||
elseif(_cpu_model EQUAL 85) # 55
|
||||
set(TARGET_ARCHITECTURE "skylake-avx512")
|
||||
elseif(_cpu_model EQUAL 78 OR _cpu_model EQUAL 94) # 4E, 5E
|
||||
set(TARGET_ARCHITECTURE "skylake")
|
||||
elseif(_cpu_model EQUAL 61 OR _cpu_model EQUAL 71 OR _cpu_model EQUAL 79 OR _cpu_model EQUAL 86) # 3D, 47, 4F, 56
|
||||
set(TARGET_ARCHITECTURE "broadwell")
|
||||
elseif(_cpu_model EQUAL 60 OR _cpu_model EQUAL 69 OR _cpu_model EQUAL 70 OR _cpu_model EQUAL 63)
|
||||
set(TARGET_ARCHITECTURE "haswell")
|
||||
elseif(_cpu_model EQUAL 58 OR _cpu_model EQUAL 62)
|
||||
set(TARGET_ARCHITECTURE "ivy-bridge")
|
||||
elseif(_cpu_model EQUAL 42 OR _cpu_model EQUAL 45)
|
||||
set(TARGET_ARCHITECTURE "sandy-bridge")
|
||||
elseif(_cpu_model EQUAL 37 OR _cpu_model EQUAL 44 OR _cpu_model EQUAL 47)
|
||||
set(TARGET_ARCHITECTURE "westmere")
|
||||
elseif(_cpu_model EQUAL 26 OR _cpu_model EQUAL 30 OR _cpu_model EQUAL 31 OR _cpu_model EQUAL 46)
|
||||
set(TARGET_ARCHITECTURE "nehalem")
|
||||
elseif(_cpu_model EQUAL 23 OR _cpu_model EQUAL 29)
|
||||
set(TARGET_ARCHITECTURE "penryn")
|
||||
elseif(_cpu_model EQUAL 15)
|
||||
set(TARGET_ARCHITECTURE "merom")
|
||||
elseif(_cpu_model EQUAL 28)
|
||||
set(TARGET_ARCHITECTURE "atom")
|
||||
elseif(_cpu_model EQUAL 14)
|
||||
set(TARGET_ARCHITECTURE "core")
|
||||
elseif(_cpu_model LESS 14)
|
||||
message(WARNING "Your CPU (family ${_cpu_family}, model ${_cpu_model}) is not known. Auto-detection of optimization flags failed and will use the generic CPU settings with SSE2.")
|
||||
set(TARGET_ARCHITECTURE "generic")
|
||||
else()
|
||||
message(WARNING "Your CPU (family ${_cpu_family}, model ${_cpu_model}) is not known. Auto-detection of optimization flags failed and will use the 65nm Core 2 CPU settings.")
|
||||
set(TARGET_ARCHITECTURE "merom")
|
||||
endif()
|
||||
elseif(_cpu_family EQUAL 7) # Itanium (not supported)
|
||||
message(WARNING "Your CPU (Itanium: family ${_cpu_family}, model ${_cpu_model}) is not supported by OptimizeForArchitecture.cmake.")
|
||||
elseif(_cpu_family EQUAL 15) # NetBurst
|
||||
list(APPEND _available_vector_units_list "sse" "sse2")
|
||||
if(_cpu_model GREATER 2) # Not sure whether this must be 3 or even 4 instead
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3")
|
||||
endif(_cpu_model GREATER 2)
|
||||
endif(_cpu_family EQUAL 6)
|
||||
elseif(_vendor_id STREQUAL "AuthenticAMD")
|
||||
if(_cpu_family EQUAL 23)
|
||||
set(TARGET_ARCHITECTURE "zen")
|
||||
elseif(_cpu_family EQUAL 22) # 16h
|
||||
set(TARGET_ARCHITECTURE "AMD 16h")
|
||||
elseif(_cpu_family EQUAL 21) # 15h
|
||||
if(_cpu_model LESS 2)
|
||||
set(TARGET_ARCHITECTURE "bulldozer")
|
||||
else()
|
||||
set(TARGET_ARCHITECTURE "piledriver")
|
||||
endif()
|
||||
elseif(_cpu_family EQUAL 20) # 14h
|
||||
set(TARGET_ARCHITECTURE "AMD 14h")
|
||||
elseif(_cpu_family EQUAL 18) # 12h
|
||||
elseif(_cpu_family EQUAL 16) # 10h
|
||||
set(TARGET_ARCHITECTURE "barcelona")
|
||||
elseif(_cpu_family EQUAL 15)
|
||||
set(TARGET_ARCHITECTURE "k8")
|
||||
if(_cpu_model GREATER 64) # I don't know the right number to put here. This is just a guess from the hardware I have access to
|
||||
set(TARGET_ARCHITECTURE "k8-sse3")
|
||||
endif(_cpu_model GREATER 64)
|
||||
endif()
|
||||
endif(_vendor_id STREQUAL "GenuineIntel")
|
||||
endmacro()
|
||||
|
||||
macro(OptimizeForArchitecture)
|
||||
if("${CMAKE_SYSTEM_PROCESSOR}" MATCHES "(x86|AMD64)")
|
||||
OptimizeForArchitectureX86()
|
||||
else()
|
||||
message(STATUS "No support for auto-detection of the target instruction set/extension")
|
||||
set(TARGET_ARCHITECTURE "unused" CACHE STRING "CPU architecture to optimize for. (unused)")
|
||||
endif()
|
||||
endmacro()
|
||||
|
||||
macro(OptimizeForArchitectureX86)
|
||||
set(TARGET_ARCHITECTURE "auto" CACHE STRING "CPU architecture to optimize for. \
|
||||
Using an incorrect setting here can result in crashes of the resulting binary because of invalid instructions used. \
|
||||
Setting the value to \"auto\" will try to optimize for the architecture where cmake is called. \
|
||||
Other supported values are: \"none\", \"generic\", \"core\", \"merom\" (65nm Core2), \
|
||||
\"penryn\" (45nm Core2), \"nehalem\", \"westmere\", \"sandy-bridge\", \"ivy-bridge\", \
|
||||
\"haswell\", \"broadwell\", \"skylake\", \"skylake-xeon\", \"kaby-lake\", \"cannonlake\", \"silvermont\", \
|
||||
\"goldmont\", \"knl\" (Knights Landing), \"atom\", \"k8\", \"k8-sse3\", \"barcelona\", \
|
||||
\"istanbul\", \"magny-cours\", \"bulldozer\", \"interlagos\", \"piledriver\", \
|
||||
\"AMD 14h\", \"AMD 16h\", \"zen\".")
|
||||
set(_force)
|
||||
if(NOT _last_target_arch STREQUAL "${TARGET_ARCHITECTURE}")
|
||||
message(STATUS "target changed from \"${_last_target_arch}\" to \"${TARGET_ARCHITECTURE}\"")
|
||||
set(_force FORCE)
|
||||
endif()
|
||||
set(_last_target_arch "${TARGET_ARCHITECTURE}" CACHE STRING "" FORCE)
|
||||
mark_as_advanced(_last_target_arch)
|
||||
string(TOLOWER "${TARGET_ARCHITECTURE}" TARGET_ARCHITECTURE)
|
||||
|
||||
set(_march_flag_list)
|
||||
set(_available_vector_units_list)
|
||||
|
||||
if(TARGET_ARCHITECTURE STREQUAL "auto")
|
||||
AutodetectHostArchitecture()
|
||||
message(STATUS "Detected CPU: ${TARGET_ARCHITECTURE}")
|
||||
endif(TARGET_ARCHITECTURE STREQUAL "auto")
|
||||
|
||||
macro(_nehalem)
|
||||
list(APPEND _march_flag_list "nehalem")
|
||||
list(APPEND _march_flag_list "corei7")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3" "sse4.1" "sse4.2")
|
||||
endmacro()
|
||||
macro(_westmere)
|
||||
list(APPEND _march_flag_list "westmere")
|
||||
_nehalem()
|
||||
endmacro()
|
||||
macro(_sandybridge)
|
||||
list(APPEND _march_flag_list "sandybridge")
|
||||
list(APPEND _march_flag_list "corei7-avx")
|
||||
_westmere()
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3" "sse4.1" "sse4.2" "avx")
|
||||
endmacro()
|
||||
macro(_ivybridge)
|
||||
list(APPEND _march_flag_list "ivybridge")
|
||||
list(APPEND _march_flag_list "core-avx-i")
|
||||
_sandybridge()
|
||||
list(APPEND _available_vector_units_list "rdrnd" "f16c")
|
||||
endmacro()
|
||||
macro(_haswell)
|
||||
list(APPEND _march_flag_list "haswell")
|
||||
list(APPEND _march_flag_list "core-avx2")
|
||||
_ivybridge()
|
||||
list(APPEND _available_vector_units_list "avx2" "fma" "bmi" "bmi2")
|
||||
endmacro()
|
||||
macro(_broadwell)
|
||||
list(APPEND _march_flag_list "broadwell")
|
||||
_haswell()
|
||||
endmacro()
|
||||
macro(_skylake)
|
||||
list(APPEND _march_flag_list "skylake")
|
||||
_broadwell()
|
||||
endmacro()
|
||||
macro(_skylake_avx512)
|
||||
list(APPEND _march_flag_list "skylake-avx512")
|
||||
_skylake()
|
||||
list(APPEND _available_vector_units_list "avx512f" "avx512cd" "avx512dq" "avx512bw" "avx512vl")
|
||||
endmacro()
|
||||
macro(_cannonlake)
|
||||
list(APPEND _march_flag_list "cannonlake")
|
||||
_skylake_avx512()
|
||||
list(APPEND _available_vector_units_list "avx512ifma" "avx512vbmi")
|
||||
endmacro()
|
||||
macro(_knightslanding)
|
||||
list(APPEND _march_flag_list "knl")
|
||||
_broadwell()
|
||||
list(APPEND _available_vector_units_list "avx512f" "avx512pf" "avx512er" "avx512cd")
|
||||
endmacro()
|
||||
macro(_silvermont)
|
||||
list(APPEND _march_flag_list "silvermont")
|
||||
_westmere()
|
||||
list(APPEND _available_vector_units_list "rdrnd")
|
||||
endmacro()
|
||||
macro(_goldmont)
|
||||
list(APPEND _march_flag_list "goldmont")
|
||||
_silvermont()
|
||||
endmacro()
|
||||
|
||||
if(TARGET_ARCHITECTURE STREQUAL "core")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "merom")
|
||||
list(APPEND _march_flag_list "merom")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "penryn")
|
||||
list(APPEND _march_flag_list "penryn")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3")
|
||||
message(STATUS "Sadly the Penryn architecture exists in variants with SSE4.1 and without SSE4.1.")
|
||||
if(_cpu_flags MATCHES "sse4_1")
|
||||
message(STATUS "SSE4.1: enabled (auto-detected from this computer's CPU flags)")
|
||||
list(APPEND _available_vector_units_list "sse4.1")
|
||||
else()
|
||||
message(STATUS "SSE4.1: disabled (auto-detected from this computer's CPU flags)")
|
||||
endif()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "knl")
|
||||
_knightslanding()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "cannonlake")
|
||||
_cannonlake()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "kaby-lake")
|
||||
_skylake()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "skylake-xeon" OR TARGET_ARCHITECTURE STREQUAL "skylake-avx512")
|
||||
_skylake_avx512()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "skylake")
|
||||
_skylake()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "broadwell")
|
||||
_broadwell()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "haswell")
|
||||
_haswell()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "ivy-bridge")
|
||||
_ivybridge()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "sandy-bridge")
|
||||
_sandybridge()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "westmere")
|
||||
_westmere()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "nehalem")
|
||||
_nehalem()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "goldmont")
|
||||
_goldmont()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "silvermont")
|
||||
_silvermont()
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "atom")
|
||||
list(APPEND _march_flag_list "atom")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "k8")
|
||||
list(APPEND _march_flag_list "k8")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "k8-sse3")
|
||||
list(APPEND _march_flag_list "k8-sse3")
|
||||
list(APPEND _march_flag_list "k8")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "AMD 16h")
|
||||
list(APPEND _march_flag_list "btver2")
|
||||
list(APPEND _march_flag_list "btver1")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3" "sse4a" "sse4.1" "sse4.2" "avx" "f16c")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "AMD 14h")
|
||||
list(APPEND _march_flag_list "btver1")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3" "sse4a")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "zen")
|
||||
list(APPEND _march_flag_list "znver1")
|
||||
_skylake()
|
||||
list(APPEND _available_vector_units_list "sse4a")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "piledriver")
|
||||
list(APPEND _march_flag_list "bdver2")
|
||||
list(APPEND _march_flag_list "bdver1")
|
||||
list(APPEND _march_flag_list "bulldozer")
|
||||
list(APPEND _march_flag_list "barcelona")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3" "sse4a" "sse4.1" "sse4.2" "avx" "xop" "fma4" "fma" "f16c")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "interlagos")
|
||||
list(APPEND _march_flag_list "bdver1")
|
||||
list(APPEND _march_flag_list "bulldozer")
|
||||
list(APPEND _march_flag_list "barcelona")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3" "sse4a" "sse4.1" "sse4.2" "avx" "xop" "fma4")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "bulldozer")
|
||||
list(APPEND _march_flag_list "bdver1")
|
||||
list(APPEND _march_flag_list "bulldozer")
|
||||
list(APPEND _march_flag_list "barcelona")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "ssse3" "sse4a" "sse4.1" "sse4.2" "avx" "xop" "fma4")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "barcelona")
|
||||
list(APPEND _march_flag_list "barcelona")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "sse4a")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "istanbul")
|
||||
list(APPEND _march_flag_list "barcelona")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "sse4a")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "magny-cours")
|
||||
list(APPEND _march_flag_list "barcelona")
|
||||
list(APPEND _march_flag_list "core2")
|
||||
list(APPEND _available_vector_units_list "sse" "sse2" "sse3" "sse4a")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "generic")
|
||||
list(APPEND _march_flag_list "generic")
|
||||
elseif(TARGET_ARCHITECTURE STREQUAL "none")
|
||||
# add this clause to remove it from the else clause
|
||||
else(TARGET_ARCHITECTURE STREQUAL "core")
|
||||
message(FATAL_ERROR "Unknown target architecture: \"${TARGET_ARCHITECTURE}\". Please set TARGET_ARCHITECTURE to a supported value.")
|
||||
endif(TARGET_ARCHITECTURE STREQUAL "core")
|
||||
|
||||
if(NOT TARGET_ARCHITECTURE STREQUAL "none")
|
||||
set(_disable_vector_unit_list)
|
||||
set(_enable_vector_unit_list)
|
||||
if(DEFINED Vc_AVX_INTRINSICS_BROKEN AND Vc_AVX_INTRINSICS_BROKEN)
|
||||
UserWarning("AVX disabled per default because of old/broken toolchain")
|
||||
set(_avx_broken true)
|
||||
set(_avx2_broken true)
|
||||
set(_fma4_broken true)
|
||||
set(_xop_broken true)
|
||||
else()
|
||||
set(_avx_broken false)
|
||||
if(DEFINED Vc_FMA4_INTRINSICS_BROKEN AND Vc_FMA4_INTRINSICS_BROKEN)
|
||||
UserWarning("FMA4 disabled per default because of old/broken toolchain")
|
||||
set(_fma4_broken true)
|
||||
else()
|
||||
set(_fma4_broken false)
|
||||
endif()
|
||||
if(DEFINED Vc_XOP_INTRINSICS_BROKEN AND Vc_XOP_INTRINSICS_BROKEN)
|
||||
UserWarning("XOP disabled per default because of old/broken toolchain")
|
||||
set(_xop_broken true)
|
||||
else()
|
||||
set(_xop_broken false)
|
||||
endif()
|
||||
if(DEFINED Vc_AVX2_INTRINSICS_BROKEN AND Vc_AVX2_INTRINSICS_BROKEN)
|
||||
UserWarning("AVX2 disabled per default because of old/broken toolchain")
|
||||
set(_avx2_broken true)
|
||||
else()
|
||||
set(_avx2_broken false)
|
||||
endif()
|
||||
endif()
|
||||
|
||||
macro(_enable_or_disable _name _flag _documentation _broken)
|
||||
if(_broken)
|
||||
set(_found false)
|
||||
else()
|
||||
_my_find(_available_vector_units_list "${_flag}" _found)
|
||||
endif()
|
||||
set(USE_${_name} ${_found} CACHE BOOL "${documentation}" ${_force})
|
||||
mark_as_advanced(USE_${_name})
|
||||
if(USE_${_name})
|
||||
list(APPEND _enable_vector_unit_list "${_flag}")
|
||||
else()
|
||||
list(APPEND _disable_vector_unit_list "${_flag}")
|
||||
endif()
|
||||
endmacro()
|
||||
_enable_or_disable(SSE2 "sse2" "Use SSE2. If SSE2 instructions are not enabled the SSE implementation will be disabled." false)
|
||||
_enable_or_disable(SSE3 "sse3" "Use SSE3. If SSE3 instructions are not enabled they will be emulated." false)
|
||||
_enable_or_disable(SSSE3 "ssse3" "Use SSSE3. If SSSE3 instructions are not enabled they will be emulated." false)
|
||||
_enable_or_disable(SSE4_1 "sse4.1" "Use SSE4.1. If SSE4.1 instructions are not enabled they will be emulated." false)
|
||||
_enable_or_disable(SSE4_2 "sse4.2" "Use SSE4.2. If SSE4.2 instructions are not enabled they will be emulated." false)
|
||||
_enable_or_disable(SSE4a "sse4a" "Use SSE4a. If SSE4a instructions are not enabled they will be emulated." false)
|
||||
_enable_or_disable(AVX "avx" "Use AVX. This will all floating-point vector sizes relative to SSE." _avx_broken)
|
||||
_enable_or_disable(FMA "fma" "Use FMA." _avx_broken)
|
||||
_enable_or_disable(BMI2 "bmi2" "Use BMI2." _avx_broken)
|
||||
_enable_or_disable(AVX2 "avx2" "Use AVX2. This will double all of the vector sizes relative to SSE." _avx2_broken)
|
||||
_enable_or_disable(XOP "xop" "Use XOP." _xop_broken)
|
||||
_enable_or_disable(FMA4 "fma4" "Use FMA4." _fma4_broken)
|
||||
_enable_or_disable(AVX512F "avx512f" "Use AVX512F. This will double all floating-point vector sizes relative to AVX2." false)
|
||||
_enable_or_disable(AVX512VL "avx512vl" "Use AVX512VL. This enables 128- and 256-bit vector length instructions with EVEX coding (improved write-masking & more vector registers)." _avx2_broken)
|
||||
_enable_or_disable(AVX512PF "avx512pf" "Use AVX512PF. This enables prefetch instructions for gathers and scatters." false)
|
||||
_enable_or_disable(AVX512ER "avx512er" "Use AVX512ER. This enables exponential and reciprocal instructions." false)
|
||||
_enable_or_disable(AVX512CD "avx512cd" "Use AVX512CD." false)
|
||||
_enable_or_disable(AVX512DQ "avx512dq" "Use AVX512DQ." false)
|
||||
_enable_or_disable(AVX512BW "avx512bw" "Use AVX512BW." false)
|
||||
_enable_or_disable(AVX512IFMA "avx512ifma" "Use AVX512IFMA." false)
|
||||
_enable_or_disable(AVX512VBMI "avx512vbmi" "Use AVX512VBMI." false)
|
||||
|
||||
if(MSVC)
|
||||
# MSVC on 32 bit can select /arch:SSE2 (since 2010 also /arch:AVX)
|
||||
# MSVC on 64 bit cannot select anything (should have changed with MSVC 2010)
|
||||
_my_find(_enable_vector_unit_list "avx2" _found)
|
||||
if(_found)
|
||||
AddCompilerFlag("/arch:AVX2" CXX_FLAGS Vc_ARCHITECTURE_FLAGS CXX_RESULT _found)
|
||||
endif()
|
||||
if(NOT _found)
|
||||
_my_find(_enable_vector_unit_list "avx" _found)
|
||||
if(_found)
|
||||
AddCompilerFlag("/arch:AVX" CXX_FLAGS Vc_ARCHITECTURE_FLAGS CXX_RESULT _found)
|
||||
endif()
|
||||
endif()
|
||||
if(NOT _found)
|
||||
_my_find(_enable_vector_unit_list "sse2" _found)
|
||||
if(_found)
|
||||
AddCompilerFlag("/arch:SSE2" CXX_FLAGS Vc_ARCHITECTURE_FLAGS)
|
||||
endif()
|
||||
endif()
|
||||
foreach(_flag ${_enable_vector_unit_list})
|
||||
string(TOUPPER "${_flag}" _flag)
|
||||
string(REPLACE "." "_" _flag "__${_flag}__")
|
||||
add_definitions("-D${_flag}")
|
||||
endforeach(_flag)
|
||||
elseif(CMAKE_CXX_COMPILER MATCHES "/(icpc|icc)$") # ICC (on Linux)
|
||||
set(OFA_map_knl "-xMIC-AVX512")
|
||||
set(OFA_map_cannonlake "-xCORE-AVX512")
|
||||
set(OFA_map_skylake-avx512 "-xCORE-AVX512")
|
||||
set(OFA_map_skylake "-xCORE-AVX2")
|
||||
set(OFA_map_broadwell "-xCORE-AVX2")
|
||||
set(OFA_map_haswell "-xCORE-AVX2")
|
||||
set(OFA_map_ivybridge "-xCORE-AVX-I")
|
||||
set(OFA_map_sandybridge "-xAVX")
|
||||
set(OFA_map_westmere "-xSSE4.2")
|
||||
set(OFA_map_nehalem "-xSSE4.2")
|
||||
set(OFA_map_penryn "-xSSSE3")
|
||||
set(OFA_map_merom "-xSSSE3")
|
||||
set(OFA_map_core2 "-xSSE3")
|
||||
set(_ok FALSE)
|
||||
foreach(arch ${_march_flag_list})
|
||||
if(DEFINED OFA_map_${arch})
|
||||
AddCompilerFlag(${OFA_map_${arch}} CXX_FLAGS Vc_ARCHITECTURE_FLAGS CXX_RESULT _ok)
|
||||
if(_ok)
|
||||
break()
|
||||
endif()
|
||||
endif()
|
||||
endforeach()
|
||||
if(NOT _ok)
|
||||
# This is the Intel compiler, so SSE2 is a very reasonable baseline.
|
||||
message(STATUS "Did not recognize the requested architecture flag, falling back to SSE2")
|
||||
AddCompilerFlag("-xSSE2" CXX_FLAGS Vc_ARCHITECTURE_FLAGS)
|
||||
endif()
|
||||
else() # not MSVC and not ICC => GCC, Clang, Open64
|
||||
foreach(_flag ${_march_flag_list})
|
||||
AddCompilerFlag("-march=${_flag}" CXX_RESULT _good CXX_FLAGS Vc_ARCHITECTURE_FLAGS)
|
||||
if(_good)
|
||||
break()
|
||||
endif(_good)
|
||||
endforeach(_flag)
|
||||
foreach(_flag ${_enable_vector_unit_list})
|
||||
AddCompilerFlag("-m${_flag}" CXX_RESULT _result)
|
||||
if(_result)
|
||||
set(_header FALSE)
|
||||
if(_flag STREQUAL "sse3")
|
||||
set(_header "pmmintrin.h")
|
||||
elseif(_flag STREQUAL "ssse3")
|
||||
set(_header "tmmintrin.h")
|
||||
elseif(_flag STREQUAL "sse4.1")
|
||||
set(_header "smmintrin.h")
|
||||
elseif(_flag STREQUAL "sse4.2")
|
||||
set(_header "smmintrin.h")
|
||||
elseif(_flag STREQUAL "sse4a")
|
||||
set(_header "ammintrin.h")
|
||||
elseif(_flag STREQUAL "avx")
|
||||
set(_header "immintrin.h")
|
||||
elseif(_flag STREQUAL "avx2")
|
||||
set(_header "immintrin.h")
|
||||
elseif(_flag STREQUAL "fma4")
|
||||
set(_header "x86intrin.h")
|
||||
elseif(_flag STREQUAL "xop")
|
||||
set(_header "x86intrin.h")
|
||||
endif()
|
||||
set(_resultVar "HAVE_${_header}")
|
||||
string(REPLACE "." "_" _resultVar "${_resultVar}")
|
||||
if(_header)
|
||||
CHECK_INCLUDE_FILE_CXX("${_header}" ${_resultVar} "-m${_flag}")
|
||||
if(NOT ${_resultVar})
|
||||
set(_useVar "USE_${_flag}")
|
||||
string(TOUPPER "${_useVar}" _useVar)
|
||||
string(REPLACE "." "_" _useVar "${_useVar}")
|
||||
message(STATUS "disabling ${_useVar} because ${_header} is missing")
|
||||
set(${_useVar} FALSE)
|
||||
list(APPEND _disable_vector_unit_list "${_flag}")
|
||||
endif()
|
||||
endif()
|
||||
if(NOT _header OR ${_resultVar})
|
||||
list(APPEND Vc_ARCHITECTURE_FLAGS "-m${_flag}")
|
||||
endif()
|
||||
endif()
|
||||
endforeach(_flag)
|
||||
foreach(_flag ${_disable_vector_unit_list})
|
||||
AddCompilerFlag("-mno-${_flag}" CXX_FLAGS Vc_ARCHITECTURE_FLAGS)
|
||||
endforeach(_flag)
|
||||
endif()
|
||||
endif()
|
||||
endmacro()
|
Loading…
Reference in New Issue
Block a user