1*67e74705SXin Li // RUN: %clang_cc1 %s -triple=x86_64-unknown-unknown -target-feature +sha -emit-llvm -o - | FileCheck %s
2*67e74705SXin Li
3*67e74705SXin Li // Don't include mm_malloc.h, it's system specific.
4*67e74705SXin Li #define __MM_MALLOC_H
5*67e74705SXin Li
6*67e74705SXin Li #include <immintrin.h>
7*67e74705SXin Li
test_sha1rnds4(__m128i a,__m128i b)8*67e74705SXin Li __m128i test_sha1rnds4(__m128i a, __m128i b) {
9*67e74705SXin Li // CHECK: call <4 x i32> @llvm.x86.sha1rnds4
10*67e74705SXin Li return _mm_sha1rnds4_epu32(a, b, 3);
11*67e74705SXin Li }
test_sha1nexte(__m128i a,__m128i b)12*67e74705SXin Li __m128i test_sha1nexte(__m128i a, __m128i b) {
13*67e74705SXin Li // CHECK: call <4 x i32> @llvm.x86.sha1nexte
14*67e74705SXin Li return _mm_sha1nexte_epu32(a, b);
15*67e74705SXin Li }
test_sha1msg1(__m128i a,__m128i b)16*67e74705SXin Li __m128i test_sha1msg1(__m128i a, __m128i b) {
17*67e74705SXin Li // CHECK: call <4 x i32> @llvm.x86.sha1msg1
18*67e74705SXin Li return _mm_sha1msg1_epu32(a, b);
19*67e74705SXin Li }
test_sha1msg2(__m128i a,__m128i b)20*67e74705SXin Li __m128i test_sha1msg2(__m128i a, __m128i b) {
21*67e74705SXin Li // CHECK: call <4 x i32> @llvm.x86.sha1msg2
22*67e74705SXin Li return _mm_sha1msg2_epu32(a, b);
23*67e74705SXin Li }
test_sha256rnds2(__m128i a,__m128i b,__m128i c)24*67e74705SXin Li __m128i test_sha256rnds2(__m128i a, __m128i b, __m128i c) {
25*67e74705SXin Li // CHECK: call <4 x i32> @llvm.x86.sha256rnds2
26*67e74705SXin Li return _mm_sha256rnds2_epu32(a, b, c);
27*67e74705SXin Li }
test_sha256msg1(__m128i a,__m128i b)28*67e74705SXin Li __m128i test_sha256msg1(__m128i a, __m128i b) {
29*67e74705SXin Li // CHECK: call <4 x i32> @llvm.x86.sha256msg1
30*67e74705SXin Li return _mm_sha256msg1_epu32(a, b);
31*67e74705SXin Li }
test_sha256msg2(__m128i a,__m128i b)32*67e74705SXin Li __m128i test_sha256msg2(__m128i a, __m128i b) {
33*67e74705SXin Li // CHECK: call <4 x i32> @llvm.x86.sha256msg2
34*67e74705SXin Li return _mm_sha256msg2_epu32(a, b);
35*67e74705SXin Li }
36