1/*===------------------ vaesintrin.h - VAES intrinsics ---------------------===
2 *
3 *
4 * Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
5 * See https://llvm.org/LICENSE.txt for license information.
6 * SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
7 *
8 *===-----------------------------------------------------------------------===
9 */
10#ifndef __IMMINTRIN_H
11#error "Never use <vaesintrin.h> directly; include <immintrin.h> instead."
12#endif
13
14#ifndef __VAESINTRIN_H
15#define __VAESINTRIN_H
16
17/* Default attributes for YMM forms. */
18#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("vaes"), __min_vector_width__(256)))
19
20/* Default attributes for ZMM forms. */
21#define __DEFAULT_FN_ATTRS_F __attribute__((__always_inline__, __nodebug__, __target__("avx512f,vaes"), __min_vector_width__(512)))
22
23
24static __inline__ __m256i __DEFAULT_FN_ATTRS
25 _mm256_aesenc_epi128(__m256i __A, __m256i __B)
26{
27  return (__m256i) __builtin_ia32_aesenc256((__v4di) __A,
28              (__v4di) __B);
29}
30
31static __inline__ __m512i __DEFAULT_FN_ATTRS_F
32 _mm512_aesenc_epi128(__m512i __A, __m512i __B)
33{
34  return (__m512i) __builtin_ia32_aesenc512((__v8di) __A,
35              (__v8di) __B);
36}
37
38static __inline__ __m256i __DEFAULT_FN_ATTRS
39 _mm256_aesdec_epi128(__m256i __A, __m256i __B)
40{
41  return (__m256i) __builtin_ia32_aesdec256((__v4di) __A,
42              (__v4di) __B);
43}
44
45static __inline__ __m512i __DEFAULT_FN_ATTRS_F
46 _mm512_aesdec_epi128(__m512i __A, __m512i __B)
47{
48  return (__m512i) __builtin_ia32_aesdec512((__v8di) __A,
49              (__v8di) __B);
50}
51
52static __inline__ __m256i __DEFAULT_FN_ATTRS
53 _mm256_aesenclast_epi128(__m256i __A, __m256i __B)
54{
55  return (__m256i) __builtin_ia32_aesenclast256((__v4di) __A,
56              (__v4di) __B);
57}
58
59static __inline__ __m512i __DEFAULT_FN_ATTRS_F
60 _mm512_aesenclast_epi128(__m512i __A, __m512i __B)
61{
62  return (__m512i) __builtin_ia32_aesenclast512((__v8di) __A,
63              (__v8di) __B);
64}
65
66static __inline__ __m256i __DEFAULT_FN_ATTRS
67 _mm256_aesdeclast_epi128(__m256i __A, __m256i __B)
68{
69  return (__m256i) __builtin_ia32_aesdeclast256((__v4di) __A,
70              (__v4di) __B);
71}
72
73static __inline__ __m512i __DEFAULT_FN_ATTRS_F
74 _mm512_aesdeclast_epi128(__m512i __A, __m512i __B)
75{
76  return (__m512i) __builtin_ia32_aesdeclast512((__v8di) __A,
77              (__v8di) __B);
78}
79
80
81#undef __DEFAULT_FN_ATTRS
82#undef __DEFAULT_FN_ATTRS_F
83
84#endif
85