1*0b57cec5SDimitry Andric /*===---- xsavesintrin.h - XSAVES 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 <xsavesintrin.h> directly; include <immintrin.h> instead."
12*0b57cec5SDimitry Andric #endif
13*0b57cec5SDimitry Andric
14*0b57cec5SDimitry Andric #ifndef __XSAVESINTRIN_H
15*0b57cec5SDimitry Andric #define __XSAVESINTRIN_H
16*0b57cec5SDimitry Andric
17*0b57cec5SDimitry Andric /* Define the default attributes for the functions in this file. */
18*0b57cec5SDimitry Andric #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("xsaves")))
19*0b57cec5SDimitry Andric
20*0b57cec5SDimitry Andric static __inline__ void __DEFAULT_FN_ATTRS
_xsaves(void * __p,unsigned long long __m)21*0b57cec5SDimitry Andric _xsaves(void *__p, unsigned long long __m) {
22*0b57cec5SDimitry Andric __builtin_ia32_xsaves(__p, __m);
23*0b57cec5SDimitry Andric }
24*0b57cec5SDimitry Andric
25*0b57cec5SDimitry Andric static __inline__ void __DEFAULT_FN_ATTRS
_xrstors(void * __p,unsigned long long __m)26*0b57cec5SDimitry Andric _xrstors(void *__p, unsigned long long __m) {
27*0b57cec5SDimitry Andric __builtin_ia32_xrstors(__p, __m);
28*0b57cec5SDimitry Andric }
29*0b57cec5SDimitry Andric
30*0b57cec5SDimitry Andric #ifdef __x86_64__
31*0b57cec5SDimitry Andric static __inline__ void __DEFAULT_FN_ATTRS
_xrstors64(void * __p,unsigned long long __m)32*0b57cec5SDimitry Andric _xrstors64(void *__p, unsigned long long __m) {
33*0b57cec5SDimitry Andric __builtin_ia32_xrstors64(__p, __m);
34*0b57cec5SDimitry Andric }
35*0b57cec5SDimitry Andric
36*0b57cec5SDimitry Andric static __inline__ void __DEFAULT_FN_ATTRS
_xsaves64(void * __p,unsigned long long __m)37*0b57cec5SDimitry Andric _xsaves64(void *__p, unsigned long long __m) {
38*0b57cec5SDimitry Andric __builtin_ia32_xsaves64(__p, __m);
39*0b57cec5SDimitry Andric }
40*0b57cec5SDimitry Andric #endif
41*0b57cec5SDimitry Andric
42*0b57cec5SDimitry Andric #undef __DEFAULT_FN_ATTRS
43*0b57cec5SDimitry Andric
44*0b57cec5SDimitry Andric #endif
45