clang 20.0.0git
fxsrintrin.h
Go to the documentation of this file.
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.
29static __inline__ void __DEFAULT_FN_ATTRS
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.
47static __inline__ void __DEFAULT_FN_ATTRS
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.
64static __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.
82static __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
static __inline__ uint32_t volatile uint32_t * __p
Definition: arm_acle.h:88
static __inline__ void __DEFAULT_FN_ATTRS _fxsave(void *__p)
Saves the XMM, MMX, MXCSR and x87 FPU registers into a 512-byte memory region pointed to by the input...
Definition: fxsrintrin.h:30
#define __DEFAULT_FN_ATTRS
Definition: fxsrintrin.h:17
static __inline__ void __DEFAULT_FN_ATTRS _fxrstor(void *__p)
Restores the XMM, MMX, MXCSR and x87 FPU registers from the 512-byte memory region pointed to by the ...
Definition: fxsrintrin.h:48