blob: 08b1fb1dc16a36f6a7d6a25b1a7d06447e1933f3 [file] [log] [blame]
Logan Chien2833ffb2018-10-09 10:03:24 +08001/*===---- shaintrin.h - SHA intrinsics -------------------------------------===
2 *
Logan Chiendf4f7662019-09-04 16:45:23 -07003 * 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
Logan Chien2833ffb2018-10-09 10:03:24 +08006 *
7 *===-----------------------------------------------------------------------===
8 */
9
10#ifndef __IMMINTRIN_H
11#error "Never use <shaintrin.h> directly; include <immintrin.h> instead."
12#endif
13
14#ifndef __SHAINTRIN_H
15#define __SHAINTRIN_H
16
17/* Define the default attributes for the functions in this file. */
Logan Chien55afb0a2018-10-15 10:42:14 +080018#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("sha"), __min_vector_width__(128)))
Logan Chien2833ffb2018-10-09 10:03:24 +080019
Logan Chien55afb0a2018-10-15 10:42:14 +080020#define _mm_sha1rnds4_epu32(V1, V2, M) \
21 __builtin_ia32_sha1rnds4((__v4si)(__m128i)(V1), (__v4si)(__m128i)(V2), (M))
Logan Chien2833ffb2018-10-09 10:03:24 +080022
23static __inline__ __m128i __DEFAULT_FN_ATTRS
24_mm_sha1nexte_epu32(__m128i __X, __m128i __Y)
25{
26 return (__m128i)__builtin_ia32_sha1nexte((__v4si)__X, (__v4si)__Y);
27}
28
29static __inline__ __m128i __DEFAULT_FN_ATTRS
30_mm_sha1msg1_epu32(__m128i __X, __m128i __Y)
31{
32 return (__m128i)__builtin_ia32_sha1msg1((__v4si)__X, (__v4si)__Y);
33}
34
35static __inline__ __m128i __DEFAULT_FN_ATTRS
36_mm_sha1msg2_epu32(__m128i __X, __m128i __Y)
37{
38 return (__m128i)__builtin_ia32_sha1msg2((__v4si)__X, (__v4si)__Y);
39}
40
41static __inline__ __m128i __DEFAULT_FN_ATTRS
42_mm_sha256rnds2_epu32(__m128i __X, __m128i __Y, __m128i __Z)
43{
44 return (__m128i)__builtin_ia32_sha256rnds2((__v4si)__X, (__v4si)__Y, (__v4si)__Z);
45}
46
47static __inline__ __m128i __DEFAULT_FN_ATTRS
48_mm_sha256msg1_epu32(__m128i __X, __m128i __Y)
49{
50 return (__m128i)__builtin_ia32_sha256msg1((__v4si)__X, (__v4si)__Y);
51}
52
53static __inline__ __m128i __DEFAULT_FN_ATTRS
54_mm_sha256msg2_epu32(__m128i __X, __m128i __Y)
55{
56 return (__m128i)__builtin_ia32_sha256msg2((__v4si)__X, (__v4si)__Y);
57}
58
59#undef __DEFAULT_FN_ATTRS
60
61#endif /* __SHAINTRIN_H */