| // This file is part of Eigen, a lightweight C++ template library |
| // for linear algebra. |
| // |
| // Copyright (C) 2008-2015 Gael Guennebaud <gael.guennebaud@inria.fr> |
| // Copyright (C) 2006-2008 Benoit Jacob <jacob.benoit.1@gmail.com> |
| // |
| // This Source Code Form is subject to the terms of the Mozilla |
| // Public License v. 2.0. If a copy of the MPL was not distributed |
| // with this file, You can obtain one at http://mozilla.org/MPL/2.0/. |
| |
| #ifndef EIGEN_MACROS_H |
| #define EIGEN_MACROS_H |
| |
| //------------------------------------------------------------------------------------------ |
| // Eigen version and basic defaults |
| //------------------------------------------------------------------------------------------ |
| |
| #define EIGEN_WORLD_VERSION 3 |
| #define EIGEN_MAJOR_VERSION 3 |
| #define EIGEN_MINOR_VERSION 90 |
| |
| #define EIGEN_VERSION_AT_LEAST(x,y,z) (EIGEN_WORLD_VERSION>x || (EIGEN_WORLD_VERSION>=x && \ |
| (EIGEN_MAJOR_VERSION>y || (EIGEN_MAJOR_VERSION>=y && \ |
| EIGEN_MINOR_VERSION>=z)))) |
| |
| #ifdef EIGEN_DEFAULT_TO_ROW_MAJOR |
| #define EIGEN_DEFAULT_MATRIX_STORAGE_ORDER_OPTION Eigen::RowMajor |
| #else |
| #define EIGEN_DEFAULT_MATRIX_STORAGE_ORDER_OPTION Eigen::ColMajor |
| #endif |
| |
| #ifndef EIGEN_DEFAULT_DENSE_INDEX_TYPE |
| #define EIGEN_DEFAULT_DENSE_INDEX_TYPE std::ptrdiff_t |
| #endif |
| |
| // Upperbound on the C++ version to use. |
| // Expected values are 03, 11, 14, 17, etc. |
| // By default, let's use an arbitrarily large C++ version. |
| #ifndef EIGEN_MAX_CPP_VER |
| #define EIGEN_MAX_CPP_VER 99 |
| #endif |
| |
| /** Allows to disable some optimizations which might affect the accuracy of the result. |
| * Such optimization are enabled by default, and set EIGEN_FAST_MATH to 0 to disable them. |
| * They currently include: |
| * - single precision ArrayBase::sin() and ArrayBase::cos() for SSE and AVX vectorization. |
| */ |
| #ifndef EIGEN_FAST_MATH |
| #define EIGEN_FAST_MATH 1 |
| #endif |
| |
| #ifndef EIGEN_STACK_ALLOCATION_LIMIT |
| // 131072 == 128 KB |
| #define EIGEN_STACK_ALLOCATION_LIMIT 131072 |
| #endif |
| |
| //------------------------------------------------------------------------------------------ |
| // Compiler identification, EIGEN_COMP_* |
| //------------------------------------------------------------------------------------------ |
| |
| /// \internal EIGEN_COMP_GNUC set to 1 for all compilers compatible with GCC |
| #ifdef __GNUC__ |
| #define EIGEN_COMP_GNUC (__GNUC__*10+__GNUC_MINOR__) |
| #else |
| #define EIGEN_COMP_GNUC 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_CLANG set to major+minor version (e.g., 307 for clang 3.7) if the compiler is clang |
| #if defined(__clang__) |
| #define EIGEN_COMP_CLANG (__clang_major__*100+__clang_minor__) |
| #else |
| #define EIGEN_COMP_CLANG 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_CASTXML set to 1 if being preprocessed by CastXML |
| #if defined(__castxml__) |
| #define EIGEN_COMP_CASTXML 1 |
| #else |
| #define EIGEN_COMP_CASTXML 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_LLVM set to 1 if the compiler backend is llvm |
| #if defined(__llvm__) |
| #define EIGEN_COMP_LLVM 1 |
| #else |
| #define EIGEN_COMP_LLVM 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_ICC set to __INTEL_COMPILER if the compiler is Intel compiler, 0 otherwise |
| #if defined(__INTEL_COMPILER) |
| #define EIGEN_COMP_ICC __INTEL_COMPILER |
| #else |
| #define EIGEN_COMP_ICC 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_MINGW set to 1 if the compiler is mingw |
| #if defined(__MINGW32__) |
| #define EIGEN_COMP_MINGW 1 |
| #else |
| #define EIGEN_COMP_MINGW 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_SUNCC set to 1 if the compiler is Solaris Studio |
| #if defined(__SUNPRO_CC) |
| #define EIGEN_COMP_SUNCC 1 |
| #else |
| #define EIGEN_COMP_SUNCC 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_MSVC set to _MSC_VER if the compiler is Microsoft Visual C++, 0 otherwise. |
| #if defined(_MSC_VER) |
| #define EIGEN_COMP_MSVC _MSC_VER |
| #else |
| #define EIGEN_COMP_MSVC 0 |
| #endif |
| |
| #if defined(__NVCC__) |
| #if defined(__CUDACC_VER_MAJOR__) && (__CUDACC_VER_MAJOR__ >= 9) |
| #define EIGEN_COMP_NVCC ((__CUDACC_VER_MAJOR__ * 10000) + (__CUDACC_VER_MINOR__ * 100)) |
| #elif defined(__CUDACC_VER__) |
| #define EIGEN_COMP_NVCC __CUDACC_VER__ |
| #else |
| #error "NVCC did not define compiler version." |
| #endif |
| #else |
| #define EIGEN_COMP_NVCC 0 |
| #endif |
| |
| // For the record, here is a table summarizing the possible values for EIGEN_COMP_MSVC: |
| // name ver MSC_VER |
| // 2008 9 1500 |
| // 2010 10 1600 |
| // 2012 11 1700 |
| // 2013 12 1800 |
| // 2015 14 1900 |
| // "15" 15 1900 |
| // 2017-14.1 15.0 1910 |
| // 2017-14.11 15.3 1911 |
| // 2017-14.12 15.5 1912 |
| // 2017-14.13 15.6 1913 |
| // 2017-14.14 15.7 1914 |
| |
| /// \internal EIGEN_COMP_MSVC_LANG set to _MSVC_LANG if the compiler is Microsoft Visual C++, 0 otherwise. |
| #if defined(_MSVC_LANG) |
| #define EIGEN_COMP_MSVC_LANG _MSVC_LANG |
| #else |
| #define EIGEN_COMP_MSVC_LANG 0 |
| #endif |
| |
| // For the record, here is a table summarizing the possible values for EIGEN_COMP_MSVC_LANG: |
| // MSVC option Standard MSVC_LANG |
| // /std:c++14 (default as of VS 2019) C++14 201402L |
| // /std:c++17 C++17 201703L |
| // /std:c++latest >C++17 >201703L |
| |
| /// \internal EIGEN_COMP_MSVC_STRICT set to 1 if the compiler is really Microsoft Visual C++ and not ,e.g., ICC or clang-cl |
| #if EIGEN_COMP_MSVC && !(EIGEN_COMP_ICC || EIGEN_COMP_LLVM || EIGEN_COMP_CLANG) |
| #define EIGEN_COMP_MSVC_STRICT _MSC_VER |
| #else |
| #define EIGEN_COMP_MSVC_STRICT 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_IBM set to xlc version if the compiler is IBM XL C++ |
| // XLC version |
| // 3.1 0x0301 |
| // 4.5 0x0405 |
| // 5.0 0x0500 |
| // 12.1 0x0C01 |
| #if defined(__IBMCPP__) || defined(__xlc__) || defined(__ibmxl__) |
| #define EIGEN_COMP_IBM __xlC__ |
| #else |
| #define EIGEN_COMP_IBM 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_PGI set to PGI version if the compiler is Portland Group Compiler |
| #if defined(__PGI) |
| #define EIGEN_COMP_PGI (__PGIC__*100+__PGIC_MINOR__) |
| #else |
| #define EIGEN_COMP_PGI 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_ARM set to 1 if the compiler is ARM Compiler |
| #if defined(__CC_ARM) || defined(__ARMCC_VERSION) |
| #define EIGEN_COMP_ARM 1 |
| #else |
| #define EIGEN_COMP_ARM 0 |
| #endif |
| |
| /// \internal EIGEN_COMP_EMSCRIPTEN set to 1 if the compiler is Emscripten Compiler |
| #if defined(__EMSCRIPTEN__) |
| #define EIGEN_COMP_EMSCRIPTEN 1 |
| #else |
| #define EIGEN_COMP_EMSCRIPTEN 0 |
| #endif |
| |
| |
| /// \internal EIGEN_GNUC_STRICT set to 1 if the compiler is really GCC and not a compatible compiler (e.g., ICC, clang, mingw, etc.) |
| #if EIGEN_COMP_GNUC && !(EIGEN_COMP_CLANG || EIGEN_COMP_ICC || EIGEN_COMP_MINGW || EIGEN_COMP_PGI || EIGEN_COMP_IBM || EIGEN_COMP_ARM || EIGEN_COMP_EMSCRIPTEN) |
| #define EIGEN_COMP_GNUC_STRICT 1 |
| #else |
| #define EIGEN_COMP_GNUC_STRICT 0 |
| #endif |
| |
| |
| #if EIGEN_COMP_GNUC |
| #define EIGEN_GNUC_AT_LEAST(x,y) ((__GNUC__==x && __GNUC_MINOR__>=y) || __GNUC__>x) |
| #define EIGEN_GNUC_AT_MOST(x,y) ((__GNUC__==x && __GNUC_MINOR__<=y) || __GNUC__<x) |
| #define EIGEN_GNUC_AT(x,y) ( __GNUC__==x && __GNUC_MINOR__==y ) |
| #else |
| #define EIGEN_GNUC_AT_LEAST(x,y) 0 |
| #define EIGEN_GNUC_AT_MOST(x,y) 0 |
| #define EIGEN_GNUC_AT(x,y) 0 |
| #endif |
| |
| // FIXME: could probably be removed as we do not support gcc 3.x anymore |
| #if EIGEN_COMP_GNUC && (__GNUC__ <= 3) |
| #define EIGEN_GCC3_OR_OLDER 1 |
| #else |
| #define EIGEN_GCC3_OR_OLDER 0 |
| #endif |
| |
| |
| |
| //------------------------------------------------------------------------------------------ |
| // Architecture identification, EIGEN_ARCH_* |
| //------------------------------------------------------------------------------------------ |
| |
| |
| #if defined(__x86_64__) || defined(_M_X64) || defined(__amd64) |
| #define EIGEN_ARCH_x86_64 1 |
| #else |
| #define EIGEN_ARCH_x86_64 0 |
| #endif |
| |
| #if defined(__i386__) || defined(_M_IX86) || defined(_X86_) || defined(__i386) |
| #define EIGEN_ARCH_i386 1 |
| #else |
| #define EIGEN_ARCH_i386 0 |
| #endif |
| |
| #if EIGEN_ARCH_x86_64 || EIGEN_ARCH_i386 |
| #define EIGEN_ARCH_i386_OR_x86_64 1 |
| #else |
| #define EIGEN_ARCH_i386_OR_x86_64 0 |
| #endif |
| |
| /// \internal EIGEN_ARCH_ARM set to 1 if the architecture is ARM |
| #if defined(__arm__) |
| #define EIGEN_ARCH_ARM 1 |
| #else |
| #define EIGEN_ARCH_ARM 0 |
| #endif |
| |
| /// \internal EIGEN_ARCH_ARM64 set to 1 if the architecture is ARM64 |
| #if defined(__aarch64__) |
| #define EIGEN_ARCH_ARM64 1 |
| #else |
| #define EIGEN_ARCH_ARM64 0 |
| #endif |
| |
| /// \internal EIGEN_ARCH_ARM_OR_ARM64 set to 1 if the architecture is ARM or ARM64 |
| #if EIGEN_ARCH_ARM || EIGEN_ARCH_ARM64 |
| #define EIGEN_ARCH_ARM_OR_ARM64 1 |
| #else |
| #define EIGEN_ARCH_ARM_OR_ARM64 0 |
| #endif |
| |
| /// \internal EIGEN_HAS_ARM64_FP16 set to 1 if the architecture provides an IEEE |
| /// compliant Arm fp16 type |
| #if EIGEN_ARCH_ARM64 |
| #ifndef EIGEN_HAS_ARM64_FP16 |
| #if defined(__ARM_FP16_FORMAT_IEEE) |
| #define EIGEN_HAS_ARM64_FP16 1 |
| #else |
| #define EIGEN_HAS_ARM64_FP16 0 |
| #endif |
| #endif |
| #endif |
| |
| /// \internal EIGEN_HAS_ARM64_FP16_VECTOR_ARITHMETIC set to 1 if the architecture |
| /// supports Neon vector intrinsics for fp16. |
| #if EIGEN_ARCH_ARM64 |
| #ifndef EIGEN_HAS_ARM64_FP16_VECTOR_ARITHMETIC |
| #if defined(__ARM_FEATURE_FP16_VECTOR_ARITHMETIC) |
| #define EIGEN_HAS_ARM64_FP16_VECTOR_ARITHMETIC 1 |
| #else |
| #define EIGEN_HAS_ARM64_FP16_VECTOR_ARITHMETIC 0 |
| #endif |
| #endif |
| #endif |
| |
| /// \internal EIGEN_HAS_ARM64_FP16_SCALAR_ARITHMETIC set to 1 if the architecture |
| /// supports Neon scalar intrinsics for fp16. |
| #if EIGEN_ARCH_ARM64 |
| #ifndef EIGEN_HAS_ARM64_FP16_SCALAR_ARITHMETIC |
| #if defined(__ARM_FEATURE_FP16_SCALAR_ARITHMETIC) |
| #define EIGEN_HAS_ARM64_FP16_SCALAR_ARITHMETIC 1 |
| #endif |
| #endif |
| #endif |
| |
| /// \internal EIGEN_ARCH_MIPS set to 1 if the architecture is MIPS |
| #if defined(__mips__) || defined(__mips) |
| #define EIGEN_ARCH_MIPS 1 |
| #else |
| #define EIGEN_ARCH_MIPS 0 |
| #endif |
| |
| /// \internal EIGEN_ARCH_SPARC set to 1 if the architecture is SPARC |
| #if defined(__sparc__) || defined(__sparc) |
| #define EIGEN_ARCH_SPARC 1 |
| #else |
| #define EIGEN_ARCH_SPARC 0 |
| #endif |
| |
| /// \internal EIGEN_ARCH_IA64 set to 1 if the architecture is Intel Itanium |
| #if defined(__ia64__) |
| #define EIGEN_ARCH_IA64 1 |
| #else |
| #define EIGEN_ARCH_IA64 0 |
| #endif |
| |
| /// \internal EIGEN_ARCH_PPC set to 1 if the architecture is PowerPC |
| #if defined(__powerpc__) || defined(__ppc__) || defined(_M_PPC) |
| #define EIGEN_ARCH_PPC 1 |
| #else |
| #define EIGEN_ARCH_PPC 0 |
| #endif |
| |
| |
| |
| //------------------------------------------------------------------------------------------ |
| // Operating system identification, EIGEN_OS_* |
| //------------------------------------------------------------------------------------------ |
| |
| /// \internal EIGEN_OS_UNIX set to 1 if the OS is a unix variant |
| #if defined(__unix__) || defined(__unix) |
| #define EIGEN_OS_UNIX 1 |
| #else |
| #define EIGEN_OS_UNIX 0 |
| #endif |
| |
| /// \internal EIGEN_OS_LINUX set to 1 if the OS is based on Linux kernel |
| #if defined(__linux__) |
| #define EIGEN_OS_LINUX 1 |
| #else |
| #define EIGEN_OS_LINUX 0 |
| #endif |
| |
| /// \internal EIGEN_OS_ANDROID set to 1 if the OS is Android |
| // note: ANDROID is defined when using ndk_build, __ANDROID__ is defined when using a standalone toolchain. |
| #if defined(__ANDROID__) || defined(ANDROID) |
| #define EIGEN_OS_ANDROID 1 |
| #else |
| #define EIGEN_OS_ANDROID 0 |
| #endif |
| |
| /// \internal EIGEN_OS_GNULINUX set to 1 if the OS is GNU Linux and not Linux-based OS (e.g., not android) |
| #if defined(__gnu_linux__) && !(EIGEN_OS_ANDROID) |
| #define EIGEN_OS_GNULINUX 1 |
| #else |
| #define EIGEN_OS_GNULINUX 0 |
| #endif |
| |
| /// \internal EIGEN_OS_BSD set to 1 if the OS is a BSD variant |
| #if defined(__FreeBSD__) || defined(__NetBSD__) || defined(__OpenBSD__) || defined(__bsdi__) || defined(__DragonFly__) |
| #define EIGEN_OS_BSD 1 |
| #else |
| #define EIGEN_OS_BSD 0 |
| #endif |
| |
| /// \internal EIGEN_OS_MAC set to 1 if the OS is MacOS |
| #if defined(__APPLE__) |
| #define EIGEN_OS_MAC 1 |
| #else |
| #define EIGEN_OS_MAC 0 |
| #endif |
| |
| /// \internal EIGEN_OS_QNX set to 1 if the OS is QNX |
| #if defined(__QNX__) |
| #define EIGEN_OS_QNX 1 |
| #else |
| #define EIGEN_OS_QNX 0 |
| #endif |
| |
| /// \internal EIGEN_OS_WIN set to 1 if the OS is Windows based |
| #if defined(_WIN32) |
| #define EIGEN_OS_WIN 1 |
| #else |
| #define EIGEN_OS_WIN 0 |
| #endif |
| |
| /// \internal EIGEN_OS_WIN64 set to 1 if the OS is Windows 64bits |
| #if defined(_WIN64) |
| #define EIGEN_OS_WIN64 1 |
| #else |
| #define EIGEN_OS_WIN64 0 |
| #endif |
| |
| /// \internal EIGEN_OS_WINCE set to 1 if the OS is Windows CE |
| #if defined(_WIN32_WCE) |
| #define EIGEN_OS_WINCE 1 |
| #else |
| #define EIGEN_OS_WINCE 0 |
| #endif |
| |
| /// \internal EIGEN_OS_CYGWIN set to 1 if the OS is Windows/Cygwin |
| #if defined(__CYGWIN__) |
| #define EIGEN_OS_CYGWIN 1 |
| #else |
| #define EIGEN_OS_CYGWIN 0 |
| #endif |
| |
| /// \internal EIGEN_OS_WIN_STRICT set to 1 if the OS is really Windows and not some variants |
| #if EIGEN_OS_WIN && !( EIGEN_OS_WINCE || EIGEN_OS_CYGWIN ) |
| #define EIGEN_OS_WIN_STRICT 1 |
| #else |
| #define EIGEN_OS_WIN_STRICT 0 |
| #endif |
| |
| /// \internal EIGEN_OS_SUN set to __SUNPRO_C if the OS is SUN |
| // compiler solaris __SUNPRO_C |
| // version studio |
| // 5.7 10 0x570 |
| // 5.8 11 0x580 |
| // 5.9 12 0x590 |
| // 5.10 12.1 0x5100 |
| // 5.11 12.2 0x5110 |
| // 5.12 12.3 0x5120 |
| #if (defined(sun) || defined(__sun)) && !(defined(__SVR4) || defined(__svr4__)) |
| #define EIGEN_OS_SUN __SUNPRO_C |
| #else |
| #define EIGEN_OS_SUN 0 |
| #endif |
| |
| /// \internal EIGEN_OS_SOLARIS set to 1 if the OS is Solaris |
| #if (defined(sun) || defined(__sun)) && (defined(__SVR4) || defined(__svr4__)) |
| #define EIGEN_OS_SOLARIS 1 |
| #else |
| #define EIGEN_OS_SOLARIS 0 |
| #endif |
| |
| |
| //------------------------------------------------------------------------------------------ |
| // Detect GPU compilers and architectures |
| //------------------------------------------------------------------------------------------ |
| |
| // NVCC is not supported as the target platform for HIPCC |
| // Note that this also makes EIGEN_CUDACC and EIGEN_HIPCC mutually exclusive |
| #if defined(__NVCC__) && defined(__HIPCC__) |
| #error "NVCC as the target platform for HIPCC is currently not supported." |
| #endif |
| |
| #if defined(__CUDACC__) && !defined(EIGEN_NO_CUDA) |
| // Means the compiler is either nvcc or clang with CUDA enabled |
| #define EIGEN_CUDACC __CUDACC__ |
| #endif |
| |
| #if defined(__CUDA_ARCH__) && !defined(EIGEN_NO_CUDA) |
| // Means we are generating code for the device |
| #define EIGEN_CUDA_ARCH __CUDA_ARCH__ |
| #endif |
| |
| #if defined(EIGEN_CUDACC) |
| #include <cuda.h> |
| #define EIGEN_CUDA_SDK_VER (CUDA_VERSION * 10) |
| #else |
| #define EIGEN_CUDA_SDK_VER 0 |
| #endif |
| |
| #if defined(__HIPCC__) && !defined(EIGEN_NO_HIP) |
| // Means the compiler is HIPCC (analogous to EIGEN_CUDACC, but for HIP) |
| #define EIGEN_HIPCC __HIPCC__ |
| |
| // We need to include hip_runtime.h here because it pulls in |
| // ++ hip_common.h which contains the define for __HIP_DEVICE_COMPILE__ |
| // ++ host_defines.h which contains the defines for the __host__ and __device__ macros |
| #include <hip/hip_runtime.h> |
| |
| #if defined(__HIP_DEVICE_COMPILE__) |
| // analogous to EIGEN_CUDA_ARCH, but for HIP |
| #define EIGEN_HIP_DEVICE_COMPILE __HIP_DEVICE_COMPILE__ |
| #endif |
| |
| // For HIP (ROCm 3.5 and higher), we need to explicitly set the launch_bounds attribute |
| // value to 1024. The compiler assigns a default value of 256 when the attribute is not |
| // specified. This results in failures on the HIP platform, for cases when a GPU kernel |
| // without an explicit launch_bounds attribute is called with a threads_per_block value |
| // greater than 256. |
| // |
| // This is a regression in functioanlity and is expected to be fixed within the next |
| // couple of ROCm releases (compiler will go back to using 1024 value as the default) |
| // |
| // In the meantime, we will use a "only enabled for HIP" macro to set the launch_bounds |
| // attribute. |
| |
| #define EIGEN_HIP_LAUNCH_BOUNDS_1024 __launch_bounds__(1024) |
| |
| #endif |
| |
| #if !defined(EIGEN_HIP_LAUNCH_BOUNDS_1024) |
| #define EIGEN_HIP_LAUNCH_BOUNDS_1024 |
| #endif // !defined(EIGEN_HIP_LAUNCH_BOUNDS_1024) |
| |
| // Unify CUDA/HIPCC |
| |
| #if defined(EIGEN_CUDACC) || defined(EIGEN_HIPCC) |
| // |
| // If either EIGEN_CUDACC or EIGEN_HIPCC is defined, then define EIGEN_GPUCC |
| // |
| #define EIGEN_GPUCC |
| // |
| // EIGEN_HIPCC implies the HIP compiler and is used to tweak Eigen code for use in HIP kernels |
| // EIGEN_CUDACC implies the CUDA compiler and is used to tweak Eigen code for use in CUDA kernels |
| // |
| // In most cases the same tweaks are required to the Eigen code to enable in both the HIP and CUDA kernels. |
| // For those cases, the corresponding code should be guarded with |
| // #if defined(EIGEN_GPUCC) |
| // instead of |
| // #if defined(EIGEN_CUDACC) || defined(EIGEN_HIPCC) |
| // |
| // For cases where the tweak is specific to HIP, the code should be guarded with |
| // #if defined(EIGEN_HIPCC) |
| // |
| // For cases where the tweak is specific to CUDA, the code should be guarded with |
| // #if defined(EIGEN_CUDACC) |
| // |
| #endif |
| |
| #if defined(EIGEN_CUDA_ARCH) || defined(EIGEN_HIP_DEVICE_COMPILE) |
| // |
| // If either EIGEN_CUDA_ARCH or EIGEN_HIP_DEVICE_COMPILE is defined, then define EIGEN_GPU_COMPILE_PHASE |
| // |
| #define EIGEN_GPU_COMPILE_PHASE |
| // |
| // GPU compilers (HIPCC, NVCC) typically do two passes over the source code, |
| // + one to compile the source for the "host" (ie CPU) |
| // + another to compile the source for the "device" (ie. GPU) |
| // |
| // Code that needs to enabled only during the either the "host" or "device" compilation phase |
| // needs to be guarded with a macro that indicates the current compilation phase |
| // |
| // EIGEN_HIP_DEVICE_COMPILE implies the device compilation phase in HIP |
| // EIGEN_CUDA_ARCH implies the device compilation phase in CUDA |
| // |
| // In most cases, the "host" / "device" specific code is the same for both HIP and CUDA |
| // For those cases, the code should be guarded with |
| // #if defined(EIGEN_GPU_COMPILE_PHASE) |
| // instead of |
| // #if defined(EIGEN_CUDA_ARCH) || defined(EIGEN_HIP_DEVICE_COMPILE) |
| // |
| // For cases where the tweak is specific to HIP, the code should be guarded with |
| // #if defined(EIGEN_HIP_DEVICE_COMPILE) |
| // |
| // For cases where the tweak is specific to CUDA, the code should be guarded with |
| // #if defined(EIGEN_CUDA_ARCH) |
| // |
| #endif |
| |
| #if defined(EIGEN_USE_SYCL) && defined(__SYCL_DEVICE_ONLY__) |
| // EIGEN_USE_SYCL is a user-defined macro while __SYCL_DEVICE_ONLY__ is a compiler-defined macro. |
| // In most cases we want to check if both macros are defined which can be done using the define below. |
| #define SYCL_DEVICE_ONLY |
| #endif |
| |
| //------------------------------------------------------------------------------------------ |
| // Detect Compiler/Architecture/OS specific features |
| //------------------------------------------------------------------------------------------ |
| |
| #if EIGEN_GNUC_AT_MOST(4,3) && !EIGEN_COMP_CLANG |
| // see bug 89 |
| #define EIGEN_SAFE_TO_USE_STANDARD_ASSERT_MACRO 0 |
| #else |
| #define EIGEN_SAFE_TO_USE_STANDARD_ASSERT_MACRO 1 |
| #endif |
| |
| // Cross compiler wrapper around LLVM's __has_builtin |
| #ifdef __has_builtin |
| # define EIGEN_HAS_BUILTIN(x) __has_builtin(x) |
| #else |
| # define EIGEN_HAS_BUILTIN(x) 0 |
| #endif |
| |
| // A Clang feature extension to determine compiler features. |
| // We use it to determine 'cxx_rvalue_references' |
| #ifndef __has_feature |
| # define __has_feature(x) 0 |
| #endif |
| |
| // Some old compilers do not support template specializations like: |
| // template<typename T,int N> void foo(const T x[N]); |
| #if !( EIGEN_COMP_CLANG && ( (EIGEN_COMP_CLANG<309) \ |
| || (defined(__apple_build_version__) && (__apple_build_version__ < 9000000))) \ |
| || EIGEN_COMP_GNUC_STRICT && EIGEN_COMP_GNUC<49) |
| #define EIGEN_HAS_STATIC_ARRAY_TEMPLATE 1 |
| #else |
| #define EIGEN_HAS_STATIC_ARRAY_TEMPLATE 0 |
| #endif |
| |
| |
| // The macro EIGEN_COMP_CXXVER defines the c++ verson expected by the compiler. |
| // For instance, if compiling with gcc and -std=c++17, then EIGEN_COMP_CXXVER |
| // is defined to 17. |
| #if (defined(__cplusplus) && (__cplusplus > 201402L) || EIGEN_COMP_MSVC_LANG > 201402L) |
| #define EIGEN_COMP_CXXVER 17 |
| #elif (defined(__cplusplus) && (__cplusplus > 201103L) || EIGEN_COMP_MSVC >= 1910) |
| #define EIGEN_COMP_CXXVER 14 |
| #elif (defined(__cplusplus) && (__cplusplus >= 201103L) || EIGEN_COMP_MSVC >= 1900) |
| #define EIGEN_COMP_CXXVER 11 |
| #else |
| #define EIGEN_COMP_CXXVER 03 |
| #endif |
| |
| |
| // The macros EIGEN_HAS_CXX?? defines a rough estimate of available c++ features |
| // but in practice we should not rely on them but rather on the availabilty of |
| // individual features as defined later. |
| // This is why there is no EIGEN_HAS_CXX17. |
| // FIXME: get rid of EIGEN_HAS_CXX14 and maybe even EIGEN_HAS_CXX11. |
| #if EIGEN_MAX_CPP_VER>=11 && EIGEN_COMP_CXXVER>=11 |
| #define EIGEN_HAS_CXX11 1 |
| #else |
| #define EIGEN_HAS_CXX11 0 |
| #endif |
| |
| #if EIGEN_MAX_CPP_VER>=14 && EIGEN_COMP_CXXVER>=14 |
| #define EIGEN_HAS_CXX14 1 |
| #else |
| #define EIGEN_HAS_CXX14 0 |
| #endif |
| |
| // Do we support r-value references? |
| #ifndef EIGEN_HAS_RVALUE_REFERENCES |
| #if EIGEN_MAX_CPP_VER>=11 && \ |
| (__has_feature(cxx_rvalue_references) || \ |
| (defined(__cplusplus) && __cplusplus >= 201103L) || \ |
| (EIGEN_COMP_MSVC >= 1600)) |
| #define EIGEN_HAS_RVALUE_REFERENCES 1 |
| #else |
| #define EIGEN_HAS_RVALUE_REFERENCES 0 |
| #endif |
| #endif |
| |
| // Does the compiler support C99? |
| // Need to include <cmath> to make sure _GLIBCXX_USE_C99 gets defined |
| #include <cmath> |
| #ifndef EIGEN_HAS_C99_MATH |
| #if EIGEN_MAX_CPP_VER>=11 && \ |
| ((defined(__STDC_VERSION__) && (__STDC_VERSION__ >= 199901)) \ |
| || (defined(__GNUC__) && defined(_GLIBCXX_USE_C99)) \ |
| || (defined(_LIBCPP_VERSION) && !defined(_MSC_VER)) \ |
| || (EIGEN_COMP_MSVC >= 1900) || defined(SYCL_DEVICE_ONLY)) |
| #define EIGEN_HAS_C99_MATH 1 |
| #else |
| #define EIGEN_HAS_C99_MATH 0 |
| #endif |
| #endif |
| |
| // Does the compiler support result_of? |
| // It's likely that MSVC 2013 supports result_of but I couldn't not find a good source for that, |
| // so let's be conservative. |
| #ifndef EIGEN_HAS_STD_RESULT_OF |
| #if EIGEN_MAX_CPP_VER>=11 && \ |
| (__has_feature(cxx_lambdas) || (defined(__cplusplus) && __cplusplus >= 201103L) || EIGEN_COMP_MSVC >= 1900) |
| #define EIGEN_HAS_STD_RESULT_OF 1 |
| #else |
| #define EIGEN_HAS_STD_RESULT_OF 0 |
| #endif |
| #endif |
| |
| #ifndef EIGEN_HAS_ALIGNAS |
| #if EIGEN_MAX_CPP_VER>=11 && EIGEN_HAS_CXX11 && \ |
| ( __has_feature(cxx_alignas) \ |
| || EIGEN_HAS_CXX14 \ |
| || (EIGEN_COMP_MSVC >= 1800) \ |
| || (EIGEN_GNUC_AT_LEAST(4,8)) \ |
| || (EIGEN_COMP_CLANG>=305) \ |
| || (EIGEN_COMP_ICC>=1500) \ |
| || (EIGEN_COMP_PGI>=1500) \ |
| || (EIGEN_COMP_SUNCC>=0x5130)) |
| #define EIGEN_HAS_ALIGNAS 1 |
| #else |
| #define EIGEN_HAS_ALIGNAS 0 |
| #endif |
| #endif |
| |
| // Does the compiler support type_traits? |
| // - full support of type traits was added only to GCC 5.1.0. |
| // - 20150626 corresponds to the last release of 4.x libstdc++ |
| #ifndef EIGEN_HAS_TYPE_TRAITS |
| #if EIGEN_MAX_CPP_VER>=11 && (EIGEN_HAS_CXX11 || EIGEN_COMP_MSVC >= 1700) \ |
| && ((!EIGEN_COMP_GNUC_STRICT) || EIGEN_GNUC_AT_LEAST(5, 1)) \ |
| && ((!defined(__GLIBCXX__)) || __GLIBCXX__ > 20150626) |
| #define EIGEN_HAS_TYPE_TRAITS 1 |
| #define EIGEN_INCLUDE_TYPE_TRAITS |
| #else |
| #define EIGEN_HAS_TYPE_TRAITS 0 |
| #endif |
| #endif |
| |
| // Does the compiler support variadic templates? |
| #ifndef EIGEN_HAS_VARIADIC_TEMPLATES |
| #if EIGEN_MAX_CPP_VER>=11 && (__cplusplus > 199711L || EIGEN_COMP_MSVC >= 1900) \ |
| && (!defined(__NVCC__) || !EIGEN_ARCH_ARM_OR_ARM64 || (EIGEN_COMP_NVCC >= 80000) ) |
| // ^^ Disable the use of variadic templates when compiling with versions of nvcc older than 8.0 on ARM devices: |
| // this prevents nvcc from crashing when compiling Eigen on Tegra X1 |
| #define EIGEN_HAS_VARIADIC_TEMPLATES 1 |
| #elif EIGEN_MAX_CPP_VER>=11 && (__cplusplus > 199711L || EIGEN_COMP_MSVC >= 1900) && defined(SYCL_DEVICE_ONLY) |
| #define EIGEN_HAS_VARIADIC_TEMPLATES 1 |
| #else |
| #define EIGEN_HAS_VARIADIC_TEMPLATES 0 |
| #endif |
| #endif |
| |
| // Does the compiler fully support const expressions? (as in c++14) |
| #ifndef EIGEN_HAS_CONSTEXPR |
| #if defined(EIGEN_CUDACC) |
| // Const expressions are supported provided that c++11 is enabled and we're using either clang or nvcc 7.5 or above |
| #if EIGEN_MAX_CPP_VER>=14 && (__cplusplus > 199711L && (EIGEN_COMP_CLANG || EIGEN_COMP_NVCC >= 70500)) |
| #define EIGEN_HAS_CONSTEXPR 1 |
| #endif |
| #elif EIGEN_MAX_CPP_VER>=14 && (__has_feature(cxx_relaxed_constexpr) || (defined(__cplusplus) && __cplusplus >= 201402L) || \ |
| (EIGEN_GNUC_AT_LEAST(4,8) && (__cplusplus > 199711L)) || \ |
| (EIGEN_COMP_CLANG >= 306 && (__cplusplus > 199711L))) |
| #define EIGEN_HAS_CONSTEXPR 1 |
| #endif |
| |
| #ifndef EIGEN_HAS_CONSTEXPR |
| #define EIGEN_HAS_CONSTEXPR 0 |
| #endif |
| |
| #endif // EIGEN_HAS_CONSTEXPR |
| |
| #if EIGEN_HAS_CONSTEXPR |
| #define EIGEN_CONSTEXPR constexpr |
| #else |
| #define EIGEN_CONSTEXPR |
| #endif |
| |
| // Does the compiler support C++11 math? |
| // Let's be conservative and enable the default C++11 implementation only if we are sure it exists |
| #ifndef EIGEN_HAS_CXX11_MATH |
| #if EIGEN_MAX_CPP_VER>=11 && ((__cplusplus > 201103L) || (__cplusplus >= 201103L) && (EIGEN_COMP_GNUC_STRICT || EIGEN_COMP_CLANG || EIGEN_COMP_MSVC || EIGEN_COMP_ICC) \ |
| && (EIGEN_ARCH_i386_OR_x86_64) && (EIGEN_OS_GNULINUX || EIGEN_OS_WIN_STRICT || EIGEN_OS_MAC)) |
| #define EIGEN_HAS_CXX11_MATH 1 |
| #else |
| #define EIGEN_HAS_CXX11_MATH 0 |
| #endif |
| #endif |
| |
| // Does the compiler support proper C++11 containers? |
| #ifndef EIGEN_HAS_CXX11_CONTAINERS |
| #if EIGEN_MAX_CPP_VER>=11 && \ |
| ((__cplusplus > 201103L) \ |
| || ((__cplusplus >= 201103L) && (EIGEN_COMP_GNUC_STRICT || EIGEN_COMP_CLANG || EIGEN_COMP_ICC>=1400)) \ |
| || EIGEN_COMP_MSVC >= 1900) |
| #define EIGEN_HAS_CXX11_CONTAINERS 1 |
| #else |
| #define EIGEN_HAS_CXX11_CONTAINERS 0 |
| #endif |
| #endif |
| |
| // Does the compiler support C++11 noexcept? |
| #ifndef EIGEN_HAS_CXX11_NOEXCEPT |
| #if EIGEN_MAX_CPP_VER>=11 && \ |
| (__has_feature(cxx_noexcept) \ |
| || (__cplusplus > 201103L) \ |
| || ((__cplusplus >= 201103L) && (EIGEN_COMP_GNUC_STRICT || EIGEN_COMP_CLANG || EIGEN_COMP_ICC>=1400)) \ |
| || EIGEN_COMP_MSVC >= 1900) |
| #define EIGEN_HAS_CXX11_NOEXCEPT 1 |
| #else |
| #define EIGEN_HAS_CXX11_NOEXCEPT 0 |
| #endif |
| #endif |
| |
| #ifndef EIGEN_HAS_CXX11_ATOMIC |
| #if EIGEN_MAX_CPP_VER>=11 && \ |
| (__has_feature(cxx_atomic) \ |
| || (__cplusplus > 201103L) \ |
| || ((__cplusplus >= 201103L) && (EIGEN_COMP_MSVC==0 || EIGEN_COMP_MSVC >= 1700))) |
| #define EIGEN_HAS_CXX11_ATOMIC 1 |
| #else |
| #define EIGEN_HAS_CXX11_ATOMIC 0 |
| #endif |
| #endif |
| |
| #ifndef EIGEN_HAS_CXX11_OVERRIDE_FINAL |
| #if EIGEN_MAX_CPP_VER>=11 && \ |
| (__cplusplus >= 201103L || EIGEN_COMP_MSVC >= 1700) |
| #define EIGEN_HAS_CXX11_OVERRIDE_FINAL 1 |
| #else |
| #define EIGEN_HAS_CXX11_OVERRIDE_FINAL 0 |
| #endif |
| #endif |
| |
| // NOTE: the required Apple's clang version is very conservative |
| // and it could be that XCode 9 works just fine. |
| // NOTE: the MSVC version is based on https://en.cppreference.com/w/cpp/compiler_support |
| // and not tested. |
| #ifndef EIGEN_HAS_CXX17_OVERALIGN |
| #if EIGEN_MAX_CPP_VER>=17 && EIGEN_COMP_CXXVER>=17 && ( \ |
| (EIGEN_COMP_MSVC >= 1912) \ |
| || (EIGEN_GNUC_AT_LEAST(7,0)) \ |
| || ((!defined(__apple_build_version__)) && (EIGEN_COMP_CLANG>=500)) \ |
| || (( defined(__apple_build_version__)) && (__apple_build_version__>=10000000)) \ |
| ) |
| #define EIGEN_HAS_CXX17_OVERALIGN 1 |
| #else |
| #define EIGEN_HAS_CXX17_OVERALIGN 0 |
| #endif |
| #endif |
| |
| #if defined(EIGEN_CUDACC) && EIGEN_HAS_CONSTEXPR |
| // While available already with c++11, this is useful mostly starting with c++14 and relaxed constexpr rules |
| #if defined(__NVCC__) |
| // nvcc considers constexpr functions as __host__ __device__ with the option --expt-relaxed-constexpr |
| #ifdef __CUDACC_RELAXED_CONSTEXPR__ |
| #define EIGEN_CONSTEXPR_ARE_DEVICE_FUNC |
| #endif |
| #elif defined(__clang__) && defined(__CUDA__) && __has_feature(cxx_relaxed_constexpr) |
| // clang++ always considers constexpr functions as implicitly __host__ __device__ |
| #define EIGEN_CONSTEXPR_ARE_DEVICE_FUNC |
| #endif |
| #endif |
| |
| // Does the compiler support the __int128 and __uint128_t extensions for 128-bit |
| // integer arithmetic? |
| // |
| // Clang and GCC define __SIZEOF_INT128__ when these extensions are supported, |
| // but we avoid using them in certain cases: |
| // |
| // * Building using Clang for Windows, where the Clang runtime library has |
| // 128-bit support only on LP64 architectures, but Windows is LLP64. |
| #ifndef EIGEN_HAS_BUILTIN_INT128 |
| #if defined(__SIZEOF_INT128__) && !(EIGEN_OS_WIN && EIGEN_COMP_CLANG) |
| #define EIGEN_HAS_BUILTIN_INT128 1 |
| #else |
| #define EIGEN_HAS_BUILTIN_INT128 0 |
| #endif |
| #endif |
| |
| //------------------------------------------------------------------------------------------ |
| // Preprocessor programming helpers |
| //------------------------------------------------------------------------------------------ |
| |
| // This macro can be used to prevent from macro expansion, e.g.: |
| // std::max EIGEN_NOT_A_MACRO(a,b) |
| #define EIGEN_NOT_A_MACRO |
| |
| #define EIGEN_DEBUG_VAR(x) std::cerr << #x << " = " << x << std::endl; |
| |
| // concatenate two tokens |
| #define EIGEN_CAT2(a,b) a ## b |
| #define EIGEN_CAT(a,b) EIGEN_CAT2(a,b) |
| |
| #define EIGEN_COMMA , |
| |
| // convert a token to a string |
| #define EIGEN_MAKESTRING2(a) #a |
| #define EIGEN_MAKESTRING(a) EIGEN_MAKESTRING2(a) |
| |
| // EIGEN_STRONG_INLINE is a stronger version of the inline, using __forceinline on MSVC, |
| // but it still doesn't use GCC's always_inline. This is useful in (common) situations where MSVC needs forceinline |
| // but GCC is still doing fine with just inline. |
| #ifndef EIGEN_STRONG_INLINE |
| #if EIGEN_COMP_MSVC || EIGEN_COMP_ICC |
| #define EIGEN_STRONG_INLINE __forceinline |
| #else |
| #define EIGEN_STRONG_INLINE inline |
| #endif |
| #endif |
| |
| // EIGEN_ALWAYS_INLINE is the stronget, it has the effect of making the function inline and adding every possible |
| // attribute to maximize inlining. This should only be used when really necessary: in particular, |
| // it uses __attribute__((always_inline)) on GCC, which most of the time is useless and can severely harm compile times. |
| // FIXME with the always_inline attribute, |
| // gcc 3.4.x and 4.1 reports the following compilation error: |
| // Eval.h:91: sorry, unimplemented: inlining failed in call to 'const Eigen::Eval<Derived> Eigen::MatrixBase<Scalar, Derived>::eval() const' |
| // : function body not available |
| // See also bug 1367 |
| #if EIGEN_GNUC_AT_LEAST(4,2) && !defined(SYCL_DEVICE_ONLY) |
| #define EIGEN_ALWAYS_INLINE __attribute__((always_inline)) inline |
| #else |
| #define EIGEN_ALWAYS_INLINE EIGEN_STRONG_INLINE |
| #endif |
| |
| #if EIGEN_COMP_GNUC |
| #define EIGEN_DONT_INLINE __attribute__((noinline)) |
| #elif EIGEN_COMP_MSVC |
| #define EIGEN_DONT_INLINE __declspec(noinline) |
| #else |
| #define EIGEN_DONT_INLINE |
| #endif |
| |
| #if EIGEN_COMP_GNUC |
| #define EIGEN_PERMISSIVE_EXPR __extension__ |
| #else |
| #define EIGEN_PERMISSIVE_EXPR |
| #endif |
| |
| // GPU stuff |
| |
| // Disable some features when compiling with GPU compilers (NVCC/clang-cuda/SYCL/HIPCC) |
| #if defined(EIGEN_CUDACC) || defined(SYCL_DEVICE_ONLY) || defined(EIGEN_HIPCC) |
| // Do not try asserts on device code |
| #ifndef EIGEN_NO_DEBUG |
| #define EIGEN_NO_DEBUG |
| #endif |
| |
| #ifdef EIGEN_INTERNAL_DEBUGGING |
| #undef EIGEN_INTERNAL_DEBUGGING |
| #endif |
| |
| #ifdef EIGEN_EXCEPTIONS |
| #undef EIGEN_EXCEPTIONS |
| #endif |
| #endif |
| |
| #if defined(SYCL_DEVICE_ONLY) |
| #ifndef EIGEN_DONT_VECTORIZE |
| #define EIGEN_DONT_VECTORIZE |
| #endif |
| #define EIGEN_DEVICE_FUNC __attribute__((flatten)) __attribute__((always_inline)) |
| // All functions callable from CUDA/HIP code must be qualified with __device__ |
| #elif defined(EIGEN_GPUCC) |
| #define EIGEN_DEVICE_FUNC __host__ __device__ |
| #else |
| #define EIGEN_DEVICE_FUNC |
| #endif |
| |
| |
| // this macro allows to get rid of linking errors about multiply defined functions. |
| // - static is not very good because it prevents definitions from different object files to be merged. |
| // So static causes the resulting linked executable to be bloated with multiple copies of the same function. |
| // - inline is not perfect either as it unwantedly hints the compiler toward inlining the function. |
| #define EIGEN_DECLARE_FUNCTION_ALLOWING_MULTIPLE_DEFINITIONS EIGEN_DEVICE_FUNC |
| #define EIGEN_DEFINE_FUNCTION_ALLOWING_MULTIPLE_DEFINITIONS EIGEN_DEVICE_FUNC inline |
| |
| #ifdef NDEBUG |
| # ifndef EIGEN_NO_DEBUG |
| # define EIGEN_NO_DEBUG |
| # endif |
| #endif |
| |
| // eigen_plain_assert is where we implement the workaround for the assert() bug in GCC <= 4.3, see bug 89 |
| #ifdef EIGEN_NO_DEBUG |
| #ifdef SYCL_DEVICE_ONLY // used to silence the warning on SYCL device |
| #define eigen_plain_assert(x) EIGEN_UNUSED_VARIABLE(x) |
| #else |
| #define eigen_plain_assert(x) |
| #endif |
| #else |
| #if EIGEN_SAFE_TO_USE_STANDARD_ASSERT_MACRO |
| namespace Eigen { |
| namespace internal { |
| inline bool copy_bool(bool b) { return b; } |
| } |
| } |
| #define eigen_plain_assert(x) assert(x) |
| #else |
| // work around bug 89 |
| #include <cstdlib> // for abort |
| #include <iostream> // for std::cerr |
| |
| namespace Eigen { |
| namespace internal { |
| // trivial function copying a bool. Must be EIGEN_DONT_INLINE, so we implement it after including Eigen headers. |
| // see bug 89. |
| namespace { |
| EIGEN_DONT_INLINE bool copy_bool(bool b) { return b; } |
| } |
| inline void assert_fail(const char *condition, const char *function, const char *file, int line) |
| { |
| std::cerr << "assertion failed: " << condition << " in function " << function << " at " << file << ":" << line << std::endl; |
| abort(); |
| } |
| } |
| } |
| #define eigen_plain_assert(x) \ |
| do { \ |
| if(!Eigen::internal::copy_bool(x)) \ |
| Eigen::internal::assert_fail(EIGEN_MAKESTRING(x), __PRETTY_FUNCTION__, __FILE__, __LINE__); \ |
| } while(false) |
| #endif |
| #endif |
| |
| // eigen_assert can be overridden |
| #ifndef eigen_assert |
| #define eigen_assert(x) eigen_plain_assert(x) |
| #endif |
| |
| #ifdef EIGEN_INTERNAL_DEBUGGING |
| #define eigen_internal_assert(x) eigen_assert(x) |
| #else |
| #define eigen_internal_assert(x) |
| #endif |
| |
| #ifdef EIGEN_NO_DEBUG |
| #define EIGEN_ONLY_USED_FOR_DEBUG(x) EIGEN_UNUSED_VARIABLE(x) |
| #else |
| #define EIGEN_ONLY_USED_FOR_DEBUG(x) |
| #endif |
| |
| #ifndef EIGEN_NO_DEPRECATED_WARNING |
| #if EIGEN_COMP_GNUC |
| #define EIGEN_DEPRECATED __attribute__((deprecated)) |
| #elif EIGEN_COMP_MSVC |
| #define EIGEN_DEPRECATED __declspec(deprecated) |
| #else |
| #define EIGEN_DEPRECATED |
| #endif |
| #else |
| #define EIGEN_DEPRECATED |
| #endif |
| |
| #if EIGEN_COMP_GNUC |
| #define EIGEN_UNUSED __attribute__((unused)) |
| #else |
| #define EIGEN_UNUSED |
| #endif |
| |
| // Suppresses 'unused variable' warnings. |
| namespace Eigen { |
| namespace internal { |
| template<typename T> EIGEN_DEVICE_FUNC EIGEN_STRONG_INLINE void ignore_unused_variable(const T&) {} |
| } |
| } |
| #define EIGEN_UNUSED_VARIABLE(var) Eigen::internal::ignore_unused_variable(var); |
| |
| #if !defined(EIGEN_ASM_COMMENT) |
| #if EIGEN_COMP_GNUC && (EIGEN_ARCH_i386_OR_x86_64 || EIGEN_ARCH_ARM_OR_ARM64) |
| #define EIGEN_ASM_COMMENT(X) __asm__("#" X) |
| #else |
| #define EIGEN_ASM_COMMENT(X) |
| #endif |
| #endif |
| |
| |
| #if EIGEN_COMP_MSVC |
| // NOTE MSVC often gives C4127 warnings with compiletime if statements. See bug 1362. |
| // This workaround is ugly, but it does the job. |
| # define EIGEN_CONST_CONDITIONAL(cond) (void)0, cond |
| #else |
| # define EIGEN_CONST_CONDITIONAL(cond) cond |
| #endif |
| |
| #ifdef EIGEN_DONT_USE_RESTRICT_KEYWORD |
| #define EIGEN_RESTRICT |
| #endif |
| #ifndef EIGEN_RESTRICT |
| #define EIGEN_RESTRICT __restrict |
| #endif |
| |
| |
| #ifndef EIGEN_DEFAULT_IO_FORMAT |
| #ifdef EIGEN_MAKING_DOCS |
| // format used in Eigen's documentation |
| // needed to define it here as escaping characters in CMake add_definition's argument seems very problematic. |
| #define EIGEN_DEFAULT_IO_FORMAT Eigen::IOFormat(3, 0, " ", "\n", "", "") |
| #else |
| #define EIGEN_DEFAULT_IO_FORMAT Eigen::IOFormat() |
| #endif |
| #endif |
| |
| // just an empty macro ! |
| #define EIGEN_EMPTY |
| |
| |
| // When compiling CUDA/HIP device code with NVCC or HIPCC |
| // pull in math functions from the global namespace. |
| // In host mode, and when device code is compiled with clang, |
| // use the std versions. |
| #if (defined(EIGEN_CUDA_ARCH) && defined(__NVCC__)) || defined(EIGEN_HIP_DEVICE_COMPILE) |
| #define EIGEN_USING_STD(FUNC) using ::FUNC; |
| #else |
| #define EIGEN_USING_STD(FUNC) using std::FUNC; |
| #endif |
| |
| #if EIGEN_COMP_MSVC_STRICT && (EIGEN_COMP_MSVC < 1900 || EIGEN_COMP_NVCC) |
| // for older MSVC versions, as well as 1900 && CUDA 8, using the base operator is sufficient (cf Bugs 1000, 1324) |
| #define EIGEN_INHERIT_ASSIGNMENT_EQUAL_OPERATOR(Derived) \ |
| using Base::operator =; |
| #elif EIGEN_COMP_CLANG // workaround clang bug (see http://forum.kde.org/viewtopic.php?f=74&t=102653) |
| #define EIGEN_INHERIT_ASSIGNMENT_EQUAL_OPERATOR(Derived) \ |
| using Base::operator =; \ |
| EIGEN_DEVICE_FUNC EIGEN_STRONG_INLINE Derived& operator=(const Derived& other) { Base::operator=(other); return *this; } \ |
| template <typename OtherDerived> \ |
| EIGEN_DEVICE_FUNC EIGEN_STRONG_INLINE Derived& operator=(const DenseBase<OtherDerived>& other) { Base::operator=(other.derived()); return *this; } |
| #else |
| #define EIGEN_INHERIT_ASSIGNMENT_EQUAL_OPERATOR(Derived) \ |
| using Base::operator =; \ |
| EIGEN_DEVICE_FUNC EIGEN_STRONG_INLINE Derived& operator=(const Derived& other) \ |
| { \ |
| Base::operator=(other); \ |
| return *this; \ |
| } |
| #endif |
| |
| |
| /** |
| * \internal |
| * \brief Macro to explicitly define the default copy constructor. |
| * This is necessary, because the implicit definition is deprecated if the copy-assignment is overridden. |
| */ |
| #if EIGEN_HAS_CXX11 |
| #define EIGEN_DEFAULT_COPY_CONSTRUCTOR(CLASS) EIGEN_DEVICE_FUNC CLASS(const CLASS&) = default; |
| #else |
| #define EIGEN_DEFAULT_COPY_CONSTRUCTOR(CLASS) |
| #endif |
| |
| |
| |
| /** \internal |
| * \brief Macro to manually inherit assignment operators. |
| * This is necessary, because the implicitly defined assignment operator gets deleted when a custom operator= is defined. |
| * With C++11 or later this also default-implements the copy-constructor |
| */ |
| #define EIGEN_INHERIT_ASSIGNMENT_OPERATORS(Derived) \ |
| EIGEN_INHERIT_ASSIGNMENT_EQUAL_OPERATOR(Derived) \ |
| EIGEN_DEFAULT_COPY_CONSTRUCTOR(Derived) |
| |
| /** \internal |
| * \brief Macro to manually define default constructors and destructors. |
| * This is necessary when the copy constructor is re-defined. |
| * For empty helper classes this should usually be protected, to avoid accidentally creating empty objects. |
| * |
| * Hiding the default destructor lead to problems in C++03 mode together with boost::multiprecision |
| */ |
| #if EIGEN_HAS_CXX11 |
| #define EIGEN_DEFAULT_EMPTY_CONSTRUCTOR_AND_DESTRUCTOR(Derived) \ |
| EIGEN_DEVICE_FUNC Derived() = default; \ |
| EIGEN_DEVICE_FUNC ~Derived() = default; |
| #else |
| #define EIGEN_DEFAULT_EMPTY_CONSTRUCTOR_AND_DESTRUCTOR(Derived) \ |
| EIGEN_DEVICE_FUNC Derived() {}; \ |
| /* EIGEN_DEVICE_FUNC ~Derived() {}; */ |
| #endif |
| |
| |
| |
| |
| |
| /** |
| * Just a side note. Commenting within defines works only by documenting |
| * behind the object (via '!<'). Comments cannot be multi-line and thus |
| * we have these extra long lines. What is confusing doxygen over here is |
| * that we use '\' and basically have a bunch of typedefs with their |
| * documentation in a single line. |
| **/ |
| |
| #define EIGEN_GENERIC_PUBLIC_INTERFACE(Derived) \ |
| typedef typename Eigen::internal::traits<Derived>::Scalar Scalar; /*!< \brief Numeric type, e.g. float, double, int or std::complex<float>. */ \ |
| typedef typename Eigen::NumTraits<Scalar>::Real RealScalar; /*!< \brief The underlying numeric type for composed scalar types. \details In cases where Scalar is e.g. std::complex<T>, T were corresponding to RealScalar. */ \ |
| typedef typename Base::CoeffReturnType CoeffReturnType; /*!< \brief The return type for coefficient access. \details Depending on whether the object allows direct coefficient access (e.g. for a MatrixXd), this type is either 'const Scalar&' or simply 'Scalar' for objects that do not allow direct coefficient access. */ \ |
| typedef typename Eigen::internal::ref_selector<Derived>::type Nested; \ |
| typedef typename Eigen::internal::traits<Derived>::StorageKind StorageKind; \ |
| typedef typename Eigen::internal::traits<Derived>::StorageIndex StorageIndex; \ |
| enum CompileTimeTraits \ |
| { RowsAtCompileTime = Eigen::internal::traits<Derived>::RowsAtCompileTime, \ |
| ColsAtCompileTime = Eigen::internal::traits<Derived>::ColsAtCompileTime, \ |
| Flags = Eigen::internal::traits<Derived>::Flags, \ |
| SizeAtCompileTime = Base::SizeAtCompileTime, \ |
| MaxSizeAtCompileTime = Base::MaxSizeAtCompileTime, \ |
| IsVectorAtCompileTime = Base::IsVectorAtCompileTime }; \ |
| using Base::derived; \ |
| using Base::const_cast_derived; |
| |
| |
| // FIXME Maybe the EIGEN_DENSE_PUBLIC_INTERFACE could be removed as importing PacketScalar is rarely needed |
| #define EIGEN_DENSE_PUBLIC_INTERFACE(Derived) \ |
| EIGEN_GENERIC_PUBLIC_INTERFACE(Derived) \ |
| typedef typename Base::PacketScalar PacketScalar; |
| |
| |
| #define EIGEN_PLAIN_ENUM_MIN(a,b) (((int)a <= (int)b) ? (int)a : (int)b) |
| #define EIGEN_PLAIN_ENUM_MAX(a,b) (((int)a >= (int)b) ? (int)a : (int)b) |
| |
| // EIGEN_SIZE_MIN_PREFER_DYNAMIC gives the min between compile-time sizes. 0 has absolute priority, followed by 1, |
| // followed by Dynamic, followed by other finite values. The reason for giving Dynamic the priority over |
| // finite values is that min(3, Dynamic) should be Dynamic, since that could be anything between 0 and 3. |
| #define EIGEN_SIZE_MIN_PREFER_DYNAMIC(a,b) (((int)a == 0 || (int)b == 0) ? 0 \ |
| : ((int)a == 1 || (int)b == 1) ? 1 \ |
| : ((int)a == Dynamic || (int)b == Dynamic) ? Dynamic \ |
| : ((int)a <= (int)b) ? (int)a : (int)b) |
| |
| // EIGEN_SIZE_MIN_PREFER_FIXED is a variant of EIGEN_SIZE_MIN_PREFER_DYNAMIC comparing MaxSizes. The difference is that finite values |
| // now have priority over Dynamic, so that min(3, Dynamic) gives 3. Indeed, whatever the actual value is |
| // (between 0 and 3), it is not more than 3. |
| #define EIGEN_SIZE_MIN_PREFER_FIXED(a,b) (((int)a == 0 || (int)b == 0) ? 0 \ |
| : ((int)a == 1 || (int)b == 1) ? 1 \ |
| : ((int)a == Dynamic && (int)b == Dynamic) ? Dynamic \ |
| : ((int)a == Dynamic) ? (int)b \ |
| : ((int)b == Dynamic) ? (int)a \ |
| : ((int)a <= (int)b) ? (int)a : (int)b) |
| |
| // see EIGEN_SIZE_MIN_PREFER_DYNAMIC. No need for a separate variant for MaxSizes here. |
| #define EIGEN_SIZE_MAX(a,b) (((int)a == Dynamic || (int)b == Dynamic) ? Dynamic \ |
| : ((int)a >= (int)b) ? (int)a : (int)b) |
| |
| #define EIGEN_LOGICAL_XOR(a,b) (((a) || (b)) && !((a) && (b))) |
| |
| #define EIGEN_IMPLIES(a,b) (!(a) || (b)) |
| |
| #if EIGEN_HAS_BUILTIN(__builtin_expect) || EIGEN_COMP_GNUC |
| #define EIGEN_PREDICT_FALSE(x) (__builtin_expect(x, false)) |
| #define EIGEN_PREDICT_TRUE(x) (__builtin_expect(false || (x), true)) |
| #else |
| #define EIGEN_PREDICT_FALSE(x) (x) |
| #define EIGEN_PREDICT_TRUE(x) (x) |
| #endif |
| |
| // the expression type of a standard coefficient wise binary operation |
| #define EIGEN_CWISE_BINARY_RETURN_TYPE(LHS,RHS,OPNAME) \ |
| CwiseBinaryOp< \ |
| EIGEN_CAT(EIGEN_CAT(internal::scalar_,OPNAME),_op)< \ |
| typename internal::traits<LHS>::Scalar, \ |
| typename internal::traits<RHS>::Scalar \ |
| >, \ |
| const LHS, \ |
| const RHS \ |
| > |
| |
| #define EIGEN_MAKE_CWISE_BINARY_OP(METHOD,OPNAME) \ |
| template<typename OtherDerived> \ |
| EIGEN_DEVICE_FUNC EIGEN_STRONG_INLINE const EIGEN_CWISE_BINARY_RETURN_TYPE(Derived,OtherDerived,OPNAME) \ |
| (METHOD)(const EIGEN_CURRENT_STORAGE_BASE_CLASS<OtherDerived> &other) const \ |
| { \ |
| return EIGEN_CWISE_BINARY_RETURN_TYPE(Derived,OtherDerived,OPNAME)(derived(), other.derived()); \ |
| } |
| |
| #define EIGEN_SCALAR_BINARY_SUPPORTED(OPNAME,TYPEA,TYPEB) \ |
| (Eigen::internal::has_ReturnType<Eigen::ScalarBinaryOpTraits<TYPEA,TYPEB,EIGEN_CAT(EIGEN_CAT(Eigen::internal::scalar_,OPNAME),_op)<TYPEA,TYPEB> > >::value) |
| |
| #define EIGEN_EXPR_BINARYOP_SCALAR_RETURN_TYPE(EXPR,SCALAR,OPNAME) \ |
| CwiseBinaryOp<EIGEN_CAT(EIGEN_CAT(internal::scalar_,OPNAME),_op)<typename internal::traits<EXPR>::Scalar,SCALAR>, const EXPR, \ |
| const typename internal::plain_constant_type<EXPR,SCALAR>::type> |
| |
| #define EIGEN_SCALAR_BINARYOP_EXPR_RETURN_TYPE(SCALAR,EXPR,OPNAME) \ |
| CwiseBinaryOp<EIGEN_CAT(EIGEN_CAT(internal::scalar_,OPNAME),_op)<SCALAR,typename internal::traits<EXPR>::Scalar>, \ |
| const typename internal::plain_constant_type<EXPR,SCALAR>::type, const EXPR> |
| |
| // Workaround for MSVC 2010 (see ML thread "patch with compile for for MSVC 2010") |
| #if EIGEN_COMP_MSVC_STRICT && (EIGEN_COMP_MSVC_STRICT<=1600) |
| #define EIGEN_MSVC10_WORKAROUND_BINARYOP_RETURN_TYPE(X) typename internal::enable_if<true,X>::type |
| #else |
| #define EIGEN_MSVC10_WORKAROUND_BINARYOP_RETURN_TYPE(X) X |
| #endif |
| |
| #define EIGEN_MAKE_SCALAR_BINARY_OP_ONTHERIGHT(METHOD,OPNAME) \ |
| template <typename T> EIGEN_DEVICE_FUNC EIGEN_STRONG_INLINE \ |
| EIGEN_MSVC10_WORKAROUND_BINARYOP_RETURN_TYPE(const EIGEN_EXPR_BINARYOP_SCALAR_RETURN_TYPE(Derived,typename internal::promote_scalar_arg<Scalar EIGEN_COMMA T EIGEN_COMMA EIGEN_SCALAR_BINARY_SUPPORTED(OPNAME,Scalar,T)>::type,OPNAME))\ |
| (METHOD)(const T& scalar) const { \ |
| typedef typename internal::promote_scalar_arg<Scalar,T,EIGEN_SCALAR_BINARY_SUPPORTED(OPNAME,Scalar,T)>::type PromotedT; \ |
| return EIGEN_EXPR_BINARYOP_SCALAR_RETURN_TYPE(Derived,PromotedT,OPNAME)(derived(), \ |
| typename internal::plain_constant_type<Derived,PromotedT>::type(derived().rows(), derived().cols(), internal::scalar_constant_op<PromotedT>(scalar))); \ |
| } |
| |
| #define EIGEN_MAKE_SCALAR_BINARY_OP_ONTHELEFT(METHOD,OPNAME) \ |
| template <typename T> EIGEN_DEVICE_FUNC EIGEN_STRONG_INLINE friend \ |
| EIGEN_MSVC10_WORKAROUND_BINARYOP_RETURN_TYPE(const EIGEN_SCALAR_BINARYOP_EXPR_RETURN_TYPE(typename internal::promote_scalar_arg<Scalar EIGEN_COMMA T EIGEN_COMMA EIGEN_SCALAR_BINARY_SUPPORTED(OPNAME,T,Scalar)>::type,Derived,OPNAME)) \ |
| (METHOD)(const T& scalar, const StorageBaseType& matrix) { \ |
| typedef typename internal::promote_scalar_arg<Scalar,T,EIGEN_SCALAR_BINARY_SUPPORTED(OPNAME,T,Scalar)>::type PromotedT; \ |
| return EIGEN_SCALAR_BINARYOP_EXPR_RETURN_TYPE(PromotedT,Derived,OPNAME)( \ |
| typename internal::plain_constant_type<Derived,PromotedT>::type(matrix.derived().rows(), matrix.derived().cols(), internal::scalar_constant_op<PromotedT>(scalar)), matrix.derived()); \ |
| } |
| |
| #define EIGEN_MAKE_SCALAR_BINARY_OP(METHOD,OPNAME) \ |
| EIGEN_MAKE_SCALAR_BINARY_OP_ONTHELEFT(METHOD,OPNAME) \ |
| EIGEN_MAKE_SCALAR_BINARY_OP_ONTHERIGHT(METHOD,OPNAME) |
| |
| |
| #if (defined(_CPPUNWIND) || defined(__EXCEPTIONS)) && !defined(EIGEN_CUDA_ARCH) && !defined(EIGEN_EXCEPTIONS) && !defined(EIGEN_USE_SYCL) && !defined(EIGEN_HIP_DEVICE_COMPILE) |
| #define EIGEN_EXCEPTIONS |
| #endif |
| |
| |
| #ifdef EIGEN_EXCEPTIONS |
| # define EIGEN_THROW_X(X) throw X |
| # define EIGEN_THROW throw |
| # define EIGEN_TRY try |
| # define EIGEN_CATCH(X) catch (X) |
| #else |
| # if defined(EIGEN_CUDA_ARCH) |
| # define EIGEN_THROW_X(X) asm("trap;") |
| # define EIGEN_THROW asm("trap;") |
| # elif defined(EIGEN_HIP_DEVICE_COMPILE) |
| # define EIGEN_THROW_X(X) asm("s_trap 0") |
| # define EIGEN_THROW asm("s_trap 0") |
| # else |
| # define EIGEN_THROW_X(X) std::abort() |
| # define EIGEN_THROW std::abort() |
| # endif |
| # define EIGEN_TRY if (true) |
| # define EIGEN_CATCH(X) else |
| #endif |
| |
| |
| #if EIGEN_HAS_CXX11_NOEXCEPT |
| # define EIGEN_INCLUDE_TYPE_TRAITS |
| # define EIGEN_NOEXCEPT noexcept |
| # define EIGEN_NOEXCEPT_IF(x) noexcept(x) |
| # define EIGEN_NO_THROW noexcept(true) |
| # define EIGEN_EXCEPTION_SPEC(X) noexcept(false) |
| #else |
| # define EIGEN_NOEXCEPT |
| # define EIGEN_NOEXCEPT_IF(x) |
| # define EIGEN_NO_THROW throw() |
| # if EIGEN_COMP_MSVC || EIGEN_COMP_CXXVER>=17 |
| // MSVC does not support exception specifications (warning C4290), |
| // and they are deprecated in c++11 anyway. This is even an error in c++17. |
| # define EIGEN_EXCEPTION_SPEC(X) throw() |
| # else |
| # define EIGEN_EXCEPTION_SPEC(X) throw(X) |
| # endif |
| #endif |
| |
| #if EIGEN_HAS_VARIADIC_TEMPLATES |
| // The all function is used to enable a variadic version of eigen_assert which can take a parameter pack as its input. |
| namespace Eigen { |
| namespace internal { |
| |
| inline bool all(){ return true; } |
| |
| template<typename T, typename ...Ts> |
| bool all(T t, Ts ... ts){ return t && all(ts...); } |
| |
| } |
| } |
| #endif |
| |
| #if EIGEN_HAS_CXX11_OVERRIDE_FINAL |
| // provide override and final specifiers if they are available: |
| # define EIGEN_OVERRIDE override |
| # define EIGEN_FINAL final |
| #else |
| # define EIGEN_OVERRIDE |
| # define EIGEN_FINAL |
| #endif |
| |
| // Wrapping #pragma unroll in a macro since it is required for SYCL |
| #if defined(SYCL_DEVICE_ONLY) |
| #if defined(_MSC_VER) |
| #define EIGEN_UNROLL_LOOP __pragma(unroll) |
| #else |
| #define EIGEN_UNROLL_LOOP _Pragma("unroll") |
| #endif |
| #else |
| #define EIGEN_UNROLL_LOOP |
| #endif |
| |
| #endif // EIGEN_MACROS_H |