clang/test/CodeGen/AArch64/neon-sm4-sm3.c

   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 }