1 | |
2 | |
3 | |
4 | |
5 | |
6 | |
7 | |
8 | |
9 | |
10 | |
11 | |
12 | |
13 | |
14 | |
15 | |
16 | |
17 | |
18 | |
19 | |
20 | |
21 | |
22 | |
23 | |
24 | #ifndef __IMMINTRIN_H |
25 | #error "Never use <vaesintrin.h> directly; include <immintrin.h> instead." |
26 | #endif |
27 | |
28 | #ifndef __VAESINTRIN_H |
29 | #define __VAESINTRIN_H |
30 | |
31 | |
32 | #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("vaes"), __min_vector_width__(256))) |
33 | |
34 | |
35 | #define __DEFAULT_FN_ATTRS_F __attribute__((__always_inline__, __nodebug__, __target__("avx512f,vaes"), __min_vector_width__(512))) |
36 | |
37 | |
38 | static __inline__ __m256i __DEFAULT_FN_ATTRS |
39 | _mm256_aesenc_epi128(__m256i __A, __m256i __B) |
40 | { |
41 | return (__m256i) __builtin_ia32_aesenc256((__v4di) __A, |
42 | (__v4di) __B); |
43 | } |
44 | |
45 | static __inline__ __m512i __DEFAULT_FN_ATTRS_F |
46 | _mm512_aesenc_epi128(__m512i __A, __m512i __B) |
47 | { |
48 | return (__m512i) __builtin_ia32_aesenc512((__v8di) __A, |
49 | (__v8di) __B); |
50 | } |
51 | |
52 | static __inline__ __m256i __DEFAULT_FN_ATTRS |
53 | _mm256_aesdec_epi128(__m256i __A, __m256i __B) |
54 | { |
55 | return (__m256i) __builtin_ia32_aesdec256((__v4di) __A, |
56 | (__v4di) __B); |
57 | } |
58 | |
59 | static __inline__ __m512i __DEFAULT_FN_ATTRS_F |
60 | _mm512_aesdec_epi128(__m512i __A, __m512i __B) |
61 | { |
62 | return (__m512i) __builtin_ia32_aesdec512((__v8di) __A, |
63 | (__v8di) __B); |
64 | } |
65 | |
66 | static __inline__ __m256i __DEFAULT_FN_ATTRS |
67 | _mm256_aesenclast_epi128(__m256i __A, __m256i __B) |
68 | { |
69 | return (__m256i) __builtin_ia32_aesenclast256((__v4di) __A, |
70 | (__v4di) __B); |
71 | } |
72 | |
73 | static __inline__ __m512i __DEFAULT_FN_ATTRS_F |
74 | _mm512_aesenclast_epi128(__m512i __A, __m512i __B) |
75 | { |
76 | return (__m512i) __builtin_ia32_aesenclast512((__v8di) __A, |
77 | (__v8di) __B); |
78 | } |
79 | |
80 | static __inline__ __m256i __DEFAULT_FN_ATTRS |
81 | _mm256_aesdeclast_epi128(__m256i __A, __m256i __B) |
82 | { |
83 | return (__m256i) __builtin_ia32_aesdeclast256((__v4di) __A, |
84 | (__v4di) __B); |
85 | } |
86 | |
87 | static __inline__ __m512i __DEFAULT_FN_ATTRS_F |
88 | _mm512_aesdeclast_epi128(__m512i __A, __m512i __B) |
89 | { |
90 | return (__m512i) __builtin_ia32_aesdeclast512((__v8di) __A, |
91 | (__v8di) __B); |
92 | } |
93 | |
94 | |
95 | #undef __DEFAULT_FN_ATTRS |
96 | #undef __DEFAULT_FN_ATTRS_F |
97 | |
98 | #endif |
99 | |