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