blob: afee6aa976749307bc07ace87347c55d802089df [file] [log] [blame]
Logan Chien2833ffb2018-10-09 10:03:24 +08001/*===---- fxsrintrin.h - FXSR intrinsic ------------------------------------===
2 *
Logan Chiendf4f7662019-09-04 16:45:23 -07003 * 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
Logan Chien2833ffb2018-10-09 10:03:24 +08006 *
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
Logan Chien55afb0a2018-10-15 10:42:14 +080019/// 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.
Logan Chien2833ffb2018-10-09 10:03:24 +080029static __inline__ void __DEFAULT_FN_ATTRS
Logan Chien55afb0a2018-10-15 10:42:14 +080030_fxsave(void *__p)
31{
32 __builtin_ia32_fxsave(__p);
Logan Chien2833ffb2018-10-09 10:03:24 +080033}
34
Logan Chien55afb0a2018-10-15 10:42:14 +080035/// 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.
Logan Chien2833ffb2018-10-09 10:03:24 +080047static __inline__ void __DEFAULT_FN_ATTRS
Logan Chien55afb0a2018-10-15 10:42:14 +080048_fxrstor(void *__p)
49{
50 __builtin_ia32_fxrstor(__p);
Logan Chien2833ffb2018-10-09 10:03:24 +080051}
52
Logan Chien55afb0a2018-10-15 10:42:14 +080053#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.
Logan Chien2833ffb2018-10-09 10:03:24 +080064static __inline__ void __DEFAULT_FN_ATTRS
Logan Chien55afb0a2018-10-15 10:42:14 +080065_fxsave64(void *__p)
66{
67 __builtin_ia32_fxsave64(__p);
Logan Chien2833ffb2018-10-09 10:03:24 +080068}
69
Logan Chien55afb0a2018-10-15 10:42:14 +080070/// 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.
Logan Chien2833ffb2018-10-09 10:03:24 +080082static __inline__ void __DEFAULT_FN_ATTRS
Logan Chien55afb0a2018-10-15 10:42:14 +080083_fxrstor64(void *__p)
84{
85 __builtin_ia32_fxrstor64(__p);
Logan Chien2833ffb2018-10-09 10:03:24 +080086}
Logan Chien55afb0a2018-10-15 10:42:14 +080087#endif
Logan Chien2833ffb2018-10-09 10:03:24 +080088
89#undef __DEFAULT_FN_ATTRS
90
91#endif