1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
|
// RUN: %clang_cc1 -triple aarch64-linux-gnu -target-feature +neon \
// RUN: -target-feature +sm4 -emit-llvm -o - %s \
// RUN: | FileCheck %s
// RUN: not %clang_cc1 -Wno-error=implicit-function-declaration -triple aarch64-linux-gnu -target-feature +neon \
// RUN: -emit-llvm -o - %s 2>&1 | FileCheck --check-prefix=CHECK-NO-CRYPTO %s
// REQUIRES: aarch64-registered-target || arm-registered-target
#include <arm_neon.h>
void test_vsm3partw1(uint32x4_t a, uint32x4_t b, uint32x4_t c) {
// CHECK-LABEL: @test_vsm3partw1(
// CHECK-NO-CRYPTO: error: always_inline function 'vsm3partw1q_u32' requires target feature 'sm4'
// CHECK: call <4 x i32> @llvm.aarch64.crypto.sm3partw1
uint32x4_t result = vsm3partw1q_u32(a, b, c);
}
void test_vsm3partw2(uint32x4_t a, uint32x4_t b, uint32x4_t c) {
// CHECK-LABEL: @test_vsm3partw2(
// CHECK: call <4 x i32> @llvm.aarch64.crypto.sm3partw2
uint32x4_t result = vsm3partw2q_u32(a, b, c);
}
void test_vsm3ss1(uint32x4_t a, uint32x4_t b, uint32x4_t c) {
// CHECK-LABEL: @test_vsm3ss1(
// CHECK: call <4 x i32> @llvm.aarch64.crypto.sm3ss1
uint32x4_t result = vsm3ss1q_u32(a, b, c);
}
void test_vsm3tt1a(uint32x4_t a, uint32x4_t b, uint32x4_t c) {
// CHECK-LABEL: @test_vsm3tt1a(
// CHECK: call <4 x i32> @llvm.aarch64.crypto.sm3tt1a
uint32x4_t result = vsm3tt1aq_u32(a, b, c, 2);
}
void test_vsm3tt1b(uint32x4_t a, uint32x4_t b, uint32x4_t c) {
// CHECK-LABEL: @test_vsm3tt1b(
// CHECK: call <4 x i32> @llvm.aarch64.crypto.sm3tt1b
uint32x4_t result = vsm3tt1bq_u32(a, b, c, 2);
}
void test_vsm3tt2a(uint32x4_t a, uint32x4_t b, uint32x4_t c) {
// CHECK-LABEL: @test_vsm3tt2a(
// CHECK: call <4 x i32> @llvm.aarch64.crypto.sm3tt2a
uint32x4_t result = vsm3tt2aq_u32(a, b, c, 2);
}
void test_vsm3tt2b(uint32x4_t a, uint32x4_t b, uint32x4_t c) {
// CHECK-LABEL: @test_vsm3tt2b(
// CHECK: call <4 x i32> @llvm.aarch64.crypto.sm3tt2b
uint32x4_t result = vsm3tt2bq_u32(a, b, c, 2);
}
void test_vsm4e(uint32x4_t a, uint32x4_t b) {
// CHECK-LABEL: @test_vsm4e(
// CHECK: call <4 x i32> @llvm.aarch64.crypto.sm4e
uint32x4_t result = vsm4eq_u32(a, b);
}
void test_vsm4ekey(uint32x4_t a, uint32x4_t b) {
// CHECK-LABEL: @test_vsm4ekey(
// CHECK: call <4 x i32> @llvm.aarch64.crypto.sm4ekey
uint32x4_t result = vsm4ekeyq_u32(a, b);
}
|
