mirror of
https://github.com/Gericom/teak-llvm.git
synced 2025-06-19 11:35:51 -04:00
3d7ecc4618
Also fix one intrinsic that was using variable names without underscores. Fixes PR41932 llvm-svn: 361109
64 lines
1.6 KiB
C
64 lines
1.6 KiB
C
/*===---- xsaveintrin.h - XSAVE intrinsic ----------------------------------===
|
|
*
|
|
* Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
|
|
* See https://llvm.org/LICENSE.txt for license information.
|
|
* SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
|
|
*
|
|
*===-----------------------------------------------------------------------===
|
|
*/
|
|
|
|
#ifndef __IMMINTRIN_H
|
|
#error "Never use <xsaveintrin.h> directly; include <immintrin.h> instead."
|
|
#endif
|
|
|
|
#ifndef __XSAVEINTRIN_H
|
|
#define __XSAVEINTRIN_H
|
|
|
|
#ifdef _MSC_VER
|
|
#define _XCR_XFEATURE_ENABLED_MASK 0
|
|
#endif
|
|
|
|
/* Define the default attributes for the functions in this file. */
|
|
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("xsave")))
|
|
|
|
static __inline__ void __DEFAULT_FN_ATTRS
|
|
_xsave(void *__p, unsigned long long __m) {
|
|
__builtin_ia32_xsave(__p, __m);
|
|
}
|
|
|
|
static __inline__ void __DEFAULT_FN_ATTRS
|
|
_xrstor(void *__p, unsigned long long __m) {
|
|
__builtin_ia32_xrstor(__p, __m);
|
|
}
|
|
|
|
#ifndef _MSC_VER
|
|
#define _xgetbv(A) __builtin_ia32_xgetbv((long long)(A))
|
|
#define _xsetbv(A, B) __builtin_ia32_xsetbv((unsigned int)(A), (unsigned long long)(B))
|
|
#else
|
|
#ifdef __cplusplus
|
|
extern "C" {
|
|
#endif
|
|
unsigned __int64 __cdecl _xgetbv(unsigned int);
|
|
void __cdecl _xsetbv(unsigned int, unsigned __int64);
|
|
#ifdef __cplusplus
|
|
}
|
|
#endif
|
|
#endif /* _MSC_VER */
|
|
|
|
#ifdef __x86_64__
|
|
static __inline__ void __DEFAULT_FN_ATTRS
|
|
_xsave64(void *__p, unsigned long long __m) {
|
|
__builtin_ia32_xsave64(__p, __m);
|
|
}
|
|
|
|
static __inline__ void __DEFAULT_FN_ATTRS
|
|
_xrstor64(void *__p, unsigned long long __m) {
|
|
__builtin_ia32_xrstor64(__p, __m);
|
|
}
|
|
|
|
#endif
|
|
|
|
#undef __DEFAULT_FN_ATTRS
|
|
|
|
#endif
|