Warning: This file is not a C or C++ file. It does not have highlighting.
1 | /*===---- fxsrintrin.h - FXSR intrinsic ------------------------------------=== |
---|---|
2 | * |
3 | * Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions. |
4 | * See https://llvm.org/LICENSE.txt for license information. |
5 | * SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception |
6 | * |
7 | *===-----------------------------------------------------------------------=== |
8 | */ |
9 | |
10 | #ifndef __IMMINTRIN_H |
11 | #error "Never use <fxsrintrin.h> directly; include <immintrin.h> instead." |
12 | #endif |
13 | |
14 | #ifndef __FXSRINTRIN_H |
15 | #define __FXSRINTRIN_H |
16 | |
17 | #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("fxsr"))) |
18 | |
19 | /// Saves the XMM, MMX, MXCSR and x87 FPU registers into a 512-byte |
20 | /// memory region pointed to by the input parameter \a __p. |
21 | /// |
22 | /// \headerfile <x86intrin.h> |
23 | /// |
24 | /// This intrinsic corresponds to the <c> FXSAVE </c> instruction. |
25 | /// |
26 | /// \param __p |
27 | /// A pointer to a 512-byte memory region. The beginning of this memory |
28 | /// region should be aligned on a 16-byte boundary. |
29 | static __inline__ void __DEFAULT_FN_ATTRS |
30 | _fxsave(void *__p) |
31 | { |
32 | __builtin_ia32_fxsave(__p); |
33 | } |
34 | |
35 | /// Restores the XMM, MMX, MXCSR and x87 FPU registers from the 512-byte |
36 | /// memory region pointed to by the input parameter \a __p. The contents of |
37 | /// this memory region should have been written to by a previous \c _fxsave |
38 | /// or \c _fxsave64 intrinsic. |
39 | /// |
40 | /// \headerfile <x86intrin.h> |
41 | /// |
42 | /// This intrinsic corresponds to the <c> FXRSTOR </c> instruction. |
43 | /// |
44 | /// \param __p |
45 | /// A pointer to a 512-byte memory region. The beginning of this memory |
46 | /// region should be aligned on a 16-byte boundary. |
47 | static __inline__ void __DEFAULT_FN_ATTRS |
48 | _fxrstor(void *__p) |
49 | { |
50 | __builtin_ia32_fxrstor(__p); |
51 | } |
52 | |
53 | #ifdef __x86_64__ |
54 | /// Saves the XMM, MMX, MXCSR and x87 FPU registers into a 512-byte |
55 | /// memory region pointed to by the input parameter \a __p. |
56 | /// |
57 | /// \headerfile <x86intrin.h> |
58 | /// |
59 | /// This intrinsic corresponds to the <c> FXSAVE64 </c> instruction. |
60 | /// |
61 | /// \param __p |
62 | /// A pointer to a 512-byte memory region. The beginning of this memory |
63 | /// region should be aligned on a 16-byte boundary. |
64 | static __inline__ void __DEFAULT_FN_ATTRS |
65 | _fxsave64(void *__p) |
66 | { |
67 | __builtin_ia32_fxsave64(__p); |
68 | } |
69 | |
70 | /// Restores the XMM, MMX, MXCSR and x87 FPU registers from the 512-byte |
71 | /// memory region pointed to by the input parameter \a __p. The contents of |
72 | /// this memory region should have been written to by a previous \c _fxsave |
73 | /// or \c _fxsave64 intrinsic. |
74 | /// |
75 | /// \headerfile <x86intrin.h> |
76 | /// |
77 | /// This intrinsic corresponds to the <c> FXRSTOR64 </c> instruction. |
78 | /// |
79 | /// \param __p |
80 | /// A pointer to a 512-byte memory region. The beginning of this memory |
81 | /// region should be aligned on a 16-byte boundary. |
82 | static __inline__ void __DEFAULT_FN_ATTRS |
83 | _fxrstor64(void *__p) |
84 | { |
85 | __builtin_ia32_fxrstor64(__p); |
86 | } |
87 | #endif |
88 | |
89 | #undef __DEFAULT_FN_ATTRS |
90 | |
91 | #endif |
92 |
Warning: This file is not a C or C++ file. It does not have highlighting.