123456789101112131415161718192021222324252627282930313233343536373839404142434445464748495051525354555657585960616263646566676869707172737475767778798081828384858687888990919293949596979899100101102103104105106107108109110111112113114115116117118119120121122123124125126127128129130131132133134135136137138139140141142143144145146147148149150151152153154155156157158159 |
- /*
- Simple DirectMedia Layer
- Copyright (C) 1997-2024 Sam Lantinga <slouken@libsdl.org>
- This software is provided 'as-is', without any express or implied
- warranty. In no event will the authors be held liable for any damages
- arising from the use of this software.
- Permission is granted to anyone to use this software for any purpose,
- including commercial applications, and to alter it and redistribute it
- freely, subject to the following restrictions:
- 1. The origin of this software must not be misrepresented; you must not
- claim that you wrote the original software. If you use this software
- in a product, an acknowledgment in the product documentation would be
- appreciated but is not required.
- 2. Altered source versions must be plainly marked as such, and must not be
- misrepresented as being the original software.
- 3. This notice may not be removed or altered from any source distribution.
- */
- /*
- * Header file for CPU intrinsics for SDL
- */
- #ifndef SDL_intrin_h_
- #define SDL_intrin_h_
- #include <SDL3/SDL_stdinc.h>
- /* Need to do this here because intrin.h has C++ code in it */
- /* Visual Studio 2005 has a bug where intrin.h conflicts with winnt.h */
- #if defined(_MSC_VER) && (_MSC_VER >= 1500) && (defined(_M_IX86) || defined(_M_X64))
- #ifdef __clang__
- /* As of Clang 11, '_m_prefetchw' is conflicting with the winnt.h's version,
- so we define the needed '_m_prefetch' here as a pseudo-header, until the issue is fixed. */
- #ifndef __PRFCHWINTRIN_H
- #define __PRFCHWINTRIN_H
- static __inline__ void __attribute__((__always_inline__, __nodebug__))
- _m_prefetch(void *__P)
- {
- __builtin_prefetch (__P, 0, 3 /* _MM_HINT_T0 */);
- }
- #endif /* __PRFCHWINTRIN_H */
- #endif /* __clang__ */
- #include <intrin.h>
- #elif defined(__MINGW64_VERSION_MAJOR)
- #include <intrin.h>
- #if defined(__ARM_NEON) && !defined(SDL_DISABLE_NEON)
- # define SDL_NEON_INTRINSICS 1
- # include <arm_neon.h>
- #endif
- #else
- /* altivec.h redefining bool causes a number of problems, see bugs 3993 and 4392, so you need to explicitly define SDL_ENABLE_ALTIVEC to have it included. */
- #if defined(__ALTIVEC__) && defined(SDL_ENABLE_ALTIVEC)
- #define SDL_ALTIVEC_INTRINSICS 1
- #include <altivec.h>
- #endif
- #ifndef SDL_DISABLE_NEON
- # ifdef __ARM_NEON
- # define SDL_NEON_INTRINSICS 1
- # include <arm_neon.h>
- # elif defined(SDL_PLATFORM_WINDOWS)
- /* Visual Studio doesn't define __ARM_ARCH, but _M_ARM (if set, always 7), and _M_ARM64 (if set, always 1). */
- # ifdef _M_ARM
- # define SDL_NEON_INTRINSICS 1
- # include <armintr.h>
- # include <arm_neon.h>
- # define __ARM_NEON 1 /* Set __ARM_NEON so that it can be used elsewhere, at compile time */
- # endif
- # if defined (_M_ARM64)
- # define SDL_NEON_INTRINSICS 1
- # include <arm64intr.h>
- # include <arm64_neon.h>
- # define __ARM_NEON 1 /* Set __ARM_NEON so that it can be used elsewhere, at compile time */
- # define __ARM_ARCH 8
- # endif
- # endif
- #endif
- #endif /* compiler version */
- #if defined(__clang__) && defined(__has_attribute)
- # if __has_attribute(target)
- # define SDL_HAS_TARGET_ATTRIBS
- # endif
- #elif defined(__GNUC__) && (__GNUC__ + (__GNUC_MINOR__ >= 9) > 4) /* gcc >= 4.9 */
- # define SDL_HAS_TARGET_ATTRIBS
- #elif defined(__ICC) && __ICC >= 1600
- # define SDL_HAS_TARGET_ATTRIBS
- #endif
- #ifdef SDL_HAS_TARGET_ATTRIBS
- # define SDL_TARGETING(x) __attribute__((target(x)))
- #else
- # define SDL_TARGETING(x)
- #endif
- #ifdef __loongarch64
- # ifndef SDL_DISABLE_LSX
- # define SDL_LSX_INTRINSICS 1
- # include <lsxintrin.h>
- # endif
- # ifndef SDL_DISABLE_LASX
- # define SDL_LASX_INTRINSICS 1
- # include <lasxintrin.h>
- # endif
- #endif
- #if defined(__x86_64__) || defined(_M_X64) || defined(__i386__) || defined(_M_IX86)
- # if ((defined(_MSC_VER) && !defined(_M_X64)) || defined(__MMX__) || defined(SDL_HAS_TARGET_ATTRIBS)) && !defined(SDL_DISABLE_MMX)
- # define SDL_MMX_INTRINSICS 1
- # include <mmintrin.h>
- # endif
- # if (defined(_MSC_VER) || defined(__SSE__) || defined(SDL_HAS_TARGET_ATTRIBS)) && !defined(SDL_DISABLE_SSE)
- # define SDL_SSE_INTRINSICS 1
- # include <xmmintrin.h>
- # endif
- # if (defined(_MSC_VER) || defined(__SSE2__) || defined(SDL_HAS_TARGET_ATTRIBS)) && !defined(SDL_DISABLE_SSE2)
- # define SDL_SSE2_INTRINSICS 1
- # include <emmintrin.h>
- # endif
- # if (defined(_MSC_VER) || defined(__SSE3__) || defined(SDL_HAS_TARGET_ATTRIBS)) && !defined(SDL_DISABLE_SSE3)
- # define SDL_SSE3_INTRINSICS 1
- # include <pmmintrin.h>
- # endif
- # if (defined(_MSC_VER) || defined(__SSE4_1__) || defined(SDL_HAS_TARGET_ATTRIBS)) && !defined(SDL_DISABLE_SSE4_1)
- # define SDL_SSE4_1_INTRINSICS 1
- # include <smmintrin.h>
- # endif
- # if (defined(_MSC_VER) || defined(__SSE4_2__) || defined(SDL_HAS_TARGET_ATTRIBS)) && !defined(SDL_DISABLE_SSE4_2)
- # define SDL_SSE4_2_INTRINSICS 1
- # include <nmmintrin.h>
- # endif
- # if defined(__clang__) && (defined(_MSC_VER) || defined(__SCE__)) && !defined(__AVX__) && !defined(SDL_DISABLE_AVX)
- # define SDL_DISABLE_AVX /* see https://reviews.llvm.org/D20291 and https://reviews.llvm.org/D79194 */
- # endif
- # if (defined(_MSC_VER) || defined(__AVX__) || defined(SDL_HAS_TARGET_ATTRIBS)) && !defined(_M_ARM64EC) && !defined(SDL_DISABLE_AVX)
- # define SDL_AVX_INTRINSICS 1
- # include <immintrin.h>
- # endif
- # if defined(__clang__) && (defined(_MSC_VER) || defined(__SCE__)) && !defined(__AVX2__) && !defined(SDL_DISABLE_AVX2)
- # define SDL_DISABLE_AVX2 /* see https://reviews.llvm.org/D20291 and https://reviews.llvm.org/D79194 */
- # endif
- # if (defined(_MSC_VER) || defined(__AVX2__) || defined(SDL_HAS_TARGET_ATTRIBS)) && !defined(_M_ARM64EC) && !defined(SDL_DISABLE_AVX2)
- # define SDL_AVX2_INTRINSICS 1
- # include <immintrin.h>
- # endif
- # if defined(__clang__) && (defined(_MSC_VER) || defined(__SCE__)) && !defined(__AVX512F__) && !defined(SDL_DISABLE_AVX512F)
- # define SDL_DISABLE_AVX512F /* see https://reviews.llvm.org/D20291 and https://reviews.llvm.org/D79194 */
- # endif
- # if (defined(_MSC_VER) || defined(__AVX512F__) || defined(SDL_HAS_TARGET_ATTRIBS)) && !defined(_M_ARM64EC) && !defined(SDL_DISABLE_AVX512F)
- # define SDL_AVX512F_INTRINSICS 1
- # include <immintrin.h>
- # endif
- #endif /* defined(__x86_64__) || defined(_M_X64) || defined(__i386__) || defined(_M_IX86) */
- #endif /* SDL_intrin_h_ */
|