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 <shaintrin.h> directly; include <immintrin.h> instead." |
26 | #endif |
27 | |
28 | #ifndef __SHAINTRIN_H |
29 | #define __SHAINTRIN_H |
30 | |
31 | |
32 | #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("sha"), __min_vector_width__(128))) |
33 | |
34 | #define _mm_sha1rnds4_epu32(V1, V2, M) \ |
35 | __builtin_ia32_sha1rnds4((__v4si)(__m128i)(V1), (__v4si)(__m128i)(V2), (M)) |
36 | |
37 | static __inline__ __m128i __DEFAULT_FN_ATTRS |
38 | _mm_sha1nexte_epu32(__m128i __X, __m128i __Y) |
39 | { |
40 | return (__m128i)__builtin_ia32_sha1nexte((__v4si)__X, (__v4si)__Y); |
41 | } |
42 | |
43 | static __inline__ __m128i __DEFAULT_FN_ATTRS |
44 | _mm_sha1msg1_epu32(__m128i __X, __m128i __Y) |
45 | { |
46 | return (__m128i)__builtin_ia32_sha1msg1((__v4si)__X, (__v4si)__Y); |
47 | } |
48 | |
49 | static __inline__ __m128i __DEFAULT_FN_ATTRS |
50 | _mm_sha1msg2_epu32(__m128i __X, __m128i __Y) |
51 | { |
52 | return (__m128i)__builtin_ia32_sha1msg2((__v4si)__X, (__v4si)__Y); |
53 | } |
54 | |
55 | static __inline__ __m128i __DEFAULT_FN_ATTRS |
56 | _mm_sha256rnds2_epu32(__m128i __X, __m128i __Y, __m128i __Z) |
57 | { |
58 | return (__m128i)__builtin_ia32_sha256rnds2((__v4si)__X, (__v4si)__Y, (__v4si)__Z); |
59 | } |
60 | |
61 | static __inline__ __m128i __DEFAULT_FN_ATTRS |
62 | _mm_sha256msg1_epu32(__m128i __X, __m128i __Y) |
63 | { |
64 | return (__m128i)__builtin_ia32_sha256msg1((__v4si)__X, (__v4si)__Y); |
65 | } |
66 | |
67 | static __inline__ __m128i __DEFAULT_FN_ATTRS |
68 | _mm_sha256msg2_epu32(__m128i __X, __m128i __Y) |
69 | { |
70 | return (__m128i)__builtin_ia32_sha256msg2((__v4si)__X, (__v4si)__Y); |
71 | } |
72 | |
73 | #undef __DEFAULT_FN_ATTRS |
74 | |
75 | #endif |
76 | |