clang  12.0.0git
enqcmdintrin.h
Go to the documentation of this file.
1 /*===------------------ enqcmdintrin.h - enqcmd intrinsics -----------------===
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 <enqcmdintrin.h> directly; include <immintrin.h> instead."
12 #endif
13 
14 #ifndef __ENQCMDINTRIN_H
15 #define __ENQCMDINTRIN_H
16 
17 /* Define the default attributes for the functions in this file */
18 #define _DEFAULT_FN_ATTRS \
19  __attribute__((__always_inline__, __nodebug__, __target__("enqcmd")))
20 
21 /// Reads 64-byte command pointed by \a __src, formats 64-byte enqueue store
22 /// data, and performs 64-byte enqueue store to memory pointed by \a __dst.
23 /// This intrinsics may only be used in User mode.
24 ///
25 /// \headerfile <x86intrin.h>
26 ///
27 /// This intrinsics corresponds to the <c> ENQCMD </c> instruction.
28 ///
29 /// \param __dst
30 /// Pointer to the destination of the enqueue store.
31 /// \param __src
32 /// Pointer to 64-byte command data.
33 /// \returns If the command data is successfully written to \a __dst then 0 is
34 /// returned. Otherwise 1 is returned.
35 static __inline__ int _DEFAULT_FN_ATTRS
36 _enqcmd (void *__dst, const void *__src)
37 {
38  return __builtin_ia32_enqcmd(__dst, __src);
39 }
40 
41 /// Reads 64-byte command pointed by \a __src, formats 64-byte enqueue store
42 /// data, and performs 64-byte enqueue store to memory pointed by \a __dst
43 /// This intrinsic may only be used in Privileged mode.
44 ///
45 /// \headerfile <x86intrin.h>
46 ///
47 /// This intrinsics corresponds to the <c> ENQCMDS </c> instruction.
48 ///
49 /// \param __dst
50 /// Pointer to the destination of the enqueue store.
51 /// \param __src
52 /// Pointer to 64-byte command data.
53 /// \returns If the command data is successfully written to \a __dst then 0 is
54 /// returned. Otherwise 1 is returned.
55 static __inline__ int _DEFAULT_FN_ATTRS
56 _enqcmds (void *__dst, const void *__src)
57 {
58  return __builtin_ia32_enqcmds(__dst, __src);
59 }
60 
61 #undef _DEFAULT_FN_ATTRS
62 
63 #endif /* __ENQCMDINTRIN_H */
static __inline__ int _DEFAULT_FN_ATTRS _enqcmd(void *__dst, const void *__src)
Reads 64-byte command pointed by __src, formats 64-byte enqueue store data, and performs 64-byte enqu...
Definition: enqcmdintrin.h:36
static __inline__ int _DEFAULT_FN_ATTRS _enqcmds(void *__dst, const void *__src)
Reads 64-byte command pointed by __src, formats 64-byte enqueue store data, and performs 64-byte enqu...
Definition: enqcmdintrin.h:56
static __inline__ void const void * __src
Definition: movdirintrin.h:45
#define _DEFAULT_FN_ATTRS
Definition: enqcmdintrin.h:18