66 lines · c
1// RUN: %clang_cc1 -triple aarch64-linux-gnu -target-feature +neon \2// RUN: -target-feature +sm4 -emit-llvm -o - %s \3// RUN: | FileCheck %s4 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 %s7 8// REQUIRES: aarch64-registered-target || arm-registered-target9 10#include <arm_neon.h>11 12void 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.sm3partw116 uint32x4_t result = vsm3partw1q_u32(a, b, c);17}18 19void 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.sm3partw222 uint32x4_t result = vsm3partw2q_u32(a, b, c);23}24 25void 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.sm3ss128 uint32x4_t result = vsm3ss1q_u32(a, b, c);29}30 31void 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.sm3tt1a34 uint32x4_t result = vsm3tt1aq_u32(a, b, c, 2);35}36 37void 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.sm3tt1b40 uint32x4_t result = vsm3tt1bq_u32(a, b, c, 2);41}42 43void 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.sm3tt2a46 uint32x4_t result = vsm3tt2aq_u32(a, b, c, 2);47}48 49void 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.sm3tt2b52 uint32x4_t result = vsm3tt2bq_u32(a, b, c, 2);53}54 55void test_vsm4e(uint32x4_t a, uint32x4_t b) {56 // CHECK-LABEL: @test_vsm4e(57 // CHECK: call <4 x i32> @llvm.aarch64.crypto.sm4e58 uint32x4_t result = vsm4eq_u32(a, b);59}60 61void test_vsm4ekey(uint32x4_t a, uint32x4_t b) {62 // CHECK-LABEL: @test_vsm4ekey(63 // CHECK: call <4 x i32> @llvm.aarch64.crypto.sm4ekey64 uint32x4_t result = vsm4ekeyq_u32(a, b);65}66