clang
20.0.0git
lib
Headers
xsavecintrin.h
Go to the documentation of this file.
1
/*===---- xsavecintrin.h - XSAVEC 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 <xsavecintrin.h> directly; include <immintrin.h> instead."
12
#endif
13
14
#ifndef __XSAVECINTRIN_H
15
#define __XSAVECINTRIN_H
16
17
/* Define the default attributes for the functions in this file. */
18
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("xsavec"
)))
19
20
/// Performs a full or partial save of processor state to the memory at
21
/// \a __p. The exact state saved depends on the 64-bit mask \a __m and
22
/// processor control register \c XCR0.
23
///
24
/// \code{.operation}
25
/// mask[62:0] := __m[62:0] AND XCR0[62:0]
26
/// FOR i := 0 TO 62
27
/// IF mask[i] == 1
28
/// CASE (i) OF
29
/// 0: save X87 FPU state
30
/// 1: save SSE state
31
/// DEFAULT: __p.Ext_Save_Area[i] := ProcessorState[i]
32
/// FI
33
/// ENDFOR
34
/// __p.Header.XSTATE_BV[62:0] := INIT_FUNCTION(mask[62:0])
35
/// \endcode
36
///
37
/// \headerfile <immintrin.h>
38
///
39
/// This intrinsic corresponds to the \c XSAVEC instruction.
40
///
41
/// \param __p
42
/// Pointer to the save area; must be 64-byte aligned.
43
/// \param __m
44
/// A 64-bit mask indicating what state should be saved.
45
static
__inline__
void
__DEFAULT_FN_ATTRS
46
_xsavec
(
void
*
__p
,
unsigned
long
long
__m) {
47
__builtin_ia32_xsavec(
__p
, __m);
48
}
49
50
#ifdef __x86_64__
51
/// Performs a full or partial save of processor state to the memory at
52
/// \a __p. The exact state saved depends on the 64-bit mask \a __m and
53
/// processor control register \c XCR0.
54
///
55
/// \code{.operation}
56
/// mask[62:0] := __m[62:0] AND XCR0[62:0]
57
/// FOR i := 0 TO 62
58
/// IF mask[i] == 1
59
/// CASE (i) OF
60
/// 0: save X87 FPU state
61
/// 1: save SSE state
62
/// DEFAULT: __p.Ext_Save_Area[i] := ProcessorState[i]
63
/// FI
64
/// ENDFOR
65
/// __p.Header.XSTATE_BV[62:0] := INIT_FUNCTION(mask[62:0])
66
/// \endcode
67
///
68
/// \headerfile <immintrin.h>
69
///
70
/// This intrinsic corresponds to the \c XSAVEC64 instruction.
71
///
72
/// \param __p
73
/// Pointer to the save area; must be 64-byte aligned.
74
/// \param __m
75
/// A 64-bit mask indicating what state should be saved.
76
static
__inline__
void
__DEFAULT_FN_ATTRS
77
_xsavec64(
void
*
__p
,
unsigned
long
long
__m) {
78
__builtin_ia32_xsavec64(
__p
, __m);
79
}
80
#endif
81
82
#undef __DEFAULT_FN_ATTRS
83
84
#endif
__p
static __inline__ uint32_t volatile uint32_t * __p
Definition:
arm_acle.h:88
__DEFAULT_FN_ATTRS
#define __DEFAULT_FN_ATTRS
Definition:
xsavecintrin.h:18
_xsavec
static __inline__ void __DEFAULT_FN_ATTRS _xsavec(void *__p, unsigned long long __m)
Performs a full or partial save of processor state to the memory at __p.
Definition:
xsavecintrin.h:46
Generated on Wed Dec 4 2024 22:27:36 for clang by
1.9.6