1*0b57cec5SDimitry Andric /*===---- xsaveintrin.h - XSAVE intrinsic ----------------------------------===
2*0b57cec5SDimitry Andric *
3*0b57cec5SDimitry Andric * Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
4*0b57cec5SDimitry Andric * See https://llvm.org/LICENSE.txt for license information.
5*0b57cec5SDimitry Andric * SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
6*0b57cec5SDimitry Andric *
7*0b57cec5SDimitry Andric *===-----------------------------------------------------------------------===
8*0b57cec5SDimitry Andric */
9*0b57cec5SDimitry Andric
10*0b57cec5SDimitry Andric #ifndef __IMMINTRIN_H
11*0b57cec5SDimitry Andric #error "Never use <xsaveintrin.h> directly; include <immintrin.h> instead."
12*0b57cec5SDimitry Andric #endif
13*0b57cec5SDimitry Andric
14*0b57cec5SDimitry Andric #ifndef __XSAVEINTRIN_H
15*0b57cec5SDimitry Andric #define __XSAVEINTRIN_H
16*0b57cec5SDimitry Andric
17*0b57cec5SDimitry Andric #ifdef _MSC_VER
18*0b57cec5SDimitry Andric #define _XCR_XFEATURE_ENABLED_MASK 0
19*0b57cec5SDimitry Andric #endif
20*0b57cec5SDimitry Andric
21*0b57cec5SDimitry Andric /* Define the default attributes for the functions in this file. */
22*0b57cec5SDimitry Andric #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("xsave")))
23*0b57cec5SDimitry Andric
24*0b57cec5SDimitry Andric static __inline__ void __DEFAULT_FN_ATTRS
_xsave(void * __p,unsigned long long __m)25*0b57cec5SDimitry Andric _xsave(void *__p, unsigned long long __m) {
26*0b57cec5SDimitry Andric __builtin_ia32_xsave(__p, __m);
27*0b57cec5SDimitry Andric }
28*0b57cec5SDimitry Andric
29*0b57cec5SDimitry Andric static __inline__ void __DEFAULT_FN_ATTRS
_xrstor(void * __p,unsigned long long __m)30*0b57cec5SDimitry Andric _xrstor(void *__p, unsigned long long __m) {
31*0b57cec5SDimitry Andric __builtin_ia32_xrstor(__p, __m);
32*0b57cec5SDimitry Andric }
33*0b57cec5SDimitry Andric
34*0b57cec5SDimitry Andric #ifndef _MSC_VER
35*0b57cec5SDimitry Andric #define _xgetbv(A) __builtin_ia32_xgetbv((long long)(A))
36*0b57cec5SDimitry Andric #define _xsetbv(A, B) __builtin_ia32_xsetbv((unsigned int)(A), (unsigned long long)(B))
37*0b57cec5SDimitry Andric #else
38*0b57cec5SDimitry Andric #ifdef __cplusplus
39*0b57cec5SDimitry Andric extern "C" {
40*0b57cec5SDimitry Andric #endif
41*0b57cec5SDimitry Andric unsigned __int64 __cdecl _xgetbv(unsigned int);
42*0b57cec5SDimitry Andric void __cdecl _xsetbv(unsigned int, unsigned __int64);
43*0b57cec5SDimitry Andric #ifdef __cplusplus
44*0b57cec5SDimitry Andric }
45*0b57cec5SDimitry Andric #endif
46*0b57cec5SDimitry Andric #endif /* _MSC_VER */
47*0b57cec5SDimitry Andric
48*0b57cec5SDimitry Andric #ifdef __x86_64__
49*0b57cec5SDimitry Andric static __inline__ void __DEFAULT_FN_ATTRS
_xsave64(void * __p,unsigned long long __m)50*0b57cec5SDimitry Andric _xsave64(void *__p, unsigned long long __m) {
51*0b57cec5SDimitry Andric __builtin_ia32_xsave64(__p, __m);
52*0b57cec5SDimitry Andric }
53*0b57cec5SDimitry Andric
54*0b57cec5SDimitry Andric static __inline__ void __DEFAULT_FN_ATTRS
_xrstor64(void * __p,unsigned long long __m)55*0b57cec5SDimitry Andric _xrstor64(void *__p, unsigned long long __m) {
56*0b57cec5SDimitry Andric __builtin_ia32_xrstor64(__p, __m);
57*0b57cec5SDimitry Andric }
58*0b57cec5SDimitry Andric
59*0b57cec5SDimitry Andric #endif
60*0b57cec5SDimitry Andric
61*0b57cec5SDimitry Andric #undef __DEFAULT_FN_ATTRS
62*0b57cec5SDimitry Andric
63*0b57cec5SDimitry Andric #endif
64