165 lines · c
1// NOTE: Assertions have been autogenerated by utils/update_cc_test_checks.py2// RUN: %clang_cc1 -triple aarch64-linux-gnu -target-feature +neon \3// RUN: -target-feature +sha3 -emit-llvm -o - %s \4// RUN: | FileCheck %s5 6// REQUIRES: aarch64-registered-target || arm-registered-target7 8#include <arm_neon.h>9 10// CHECK-LABEL: @test_vsha512h(11// CHECK: call <2 x i64> @llvm.aarch64.crypto.sha512h12//13void test_vsha512h(uint64x2_t hash_ed, uint64x2_t hash_gf, uint64x2_t kwh_kwh2) {14 uint64x2_t result = vsha512hq_u64(hash_ed, hash_gf, kwh_kwh2);15}16 17// CHECK-LABEL: @test_vsha512h2(18// CHECK: call <2 x i64> @llvm.aarch64.crypto.sha512h219//20void test_vsha512h2(uint64x2_t sum_ab, uint64x2_t hash_c_, uint64x2_t hash_ab) {21 uint64x2_t result = vsha512h2q_u64(sum_ab, hash_c_, hash_ab);22}23 24// CHECK-LABEL: @test_vsha512su0(25// CHECK: call <2 x i64> @llvm.aarch64.crypto.sha512su026//27void test_vsha512su0(uint64x2_t w0_1, uint64x2_t w2_) {28 uint64x2_t result = vsha512su0q_u64(w0_1, w2_);29}30 31// CHECK-LABEL: @test_vsha512su1(32// CHECK: call <2 x i64> @llvm.aarch64.crypto.sha512su133//34void test_vsha512su1(uint64x2_t s01_s02, uint64x2_t w14_15, uint64x2_t w9_10) {35 uint64x2_t result = vsha512su1q_u64(s01_s02, w14_15, w9_10);36}37 38// CHECK-LABEL: @test_vrax1(39// CHECK: call <2 x i64> @llvm.aarch64.crypto.rax140//41void test_vrax1(uint64x2_t a, uint64x2_t b) {42 uint64x2_t result = vrax1q_u64(a, b);43}44 45 46// CHECK-LABEL: @test_xar(47// CHECK: call <2 x i64> @llvm.aarch64.crypto.xar48//49void test_xar(uint64x2_t a, uint64x2_t b) {50 uint64x2_t result = vxarq_u64(a, b, 10);51}52 53 54// CHECK-LABEL: @test_vbcax_u8(55// CHECK: call <16 x i8> @llvm.aarch64.crypto.bcaxu.v16i856//57void test_vbcax_u8(uint8x16_t a, uint8x16_t b, uint8x16_t c) {58 uint8x16_t result = vbcaxq_u8(a, b, c);59}60 61// CHECK-LABEL: @test_vbcax_u16(62// CHECK: call <8 x i16> @llvm.aarch64.crypto.bcaxu.v8i1663//64void test_vbcax_u16(uint16x8_t a, uint16x8_t b, uint16x8_t c) {65 uint16x8_t result = vbcaxq_u16(a, b, c);66}67 68// CHECK-LABEL: @test_vbcax_u32(69// CHECK: call <4 x i32> @llvm.aarch64.crypto.bcaxu.v4i3270//71void test_vbcax_u32(uint32x4_t a, uint32x4_t b, uint32x4_t c) {72 uint32x4_t result = vbcaxq_u32(a, b, c);73}74 75// CHECK-LABEL: @test_vbcax_u64(76// CHECK: call <2 x i64> @llvm.aarch64.crypto.bcaxu.v2i6477//78void test_vbcax_u64(uint64x2_t a, uint64x2_t b, uint64x2_t c) {79 uint64x2_t result = vbcaxq_u64(a, b, c);80}81 82// CHECK-LABEL: @test_vbcax_s8(83// CHECK: call <16 x i8> @llvm.aarch64.crypto.bcaxs.v16i884//85void test_vbcax_s8(int8x16_t a, int8x16_t b, int8x16_t c) {86 int8x16_t result = vbcaxq_s8(a, b, c);87}88 89// CHECK-LABEL: @test_vbcax_s16(90// CHECK: call <8 x i16> @llvm.aarch64.crypto.bcaxs.v8i1691//92void test_vbcax_s16(int16x8_t a, int16x8_t b, int16x8_t c) {93 int16x8_t result = vbcaxq_s16(a, b, c);94}95 96// CHECK-LABEL: @test_vbcax_s32(97// CHECK: call <4 x i32> @llvm.aarch64.crypto.bcaxs.v4i3298//99void test_vbcax_s32(int32x4_t a, int32x4_t b, int32x4_t c) {100 int32x4_t result = vbcaxq_s32(a, b, c);101}102 103// CHECK-LABEL: @test_vbcax_s64(104// CHECK: call <2 x i64> @llvm.aarch64.crypto.bcaxs.v2i64105//106void test_vbcax_s64(int64x2_t a, int64x2_t b, int64x2_t c) {107 int64x2_t result = vbcaxq_s64(a, b, c);108}109 110// CHECK-LABEL: @test_veor3_u8(111// CHECK: call <16 x i8> @llvm.aarch64.crypto.eor3u.v16i8112//113void test_veor3_u8(uint8x16_t a, uint8x16_t b, uint8x16_t c) {114 uint8x16_t result = veor3q_u8(a, b, c);115}116 117// CHECK-LABEL: @test_veor3_u16(118// CHECK: call <8 x i16> @llvm.aarch64.crypto.eor3u.v8i16119//120void test_veor3_u16(uint16x8_t a, uint16x8_t b, uint16x8_t c) {121 uint16x8_t result = veor3q_u16(a, b, c);122}123 124// CHECK-LABEL: @test_veor3_u32(125// CHECK: call <4 x i32> @llvm.aarch64.crypto.eor3u.v4i32126//127void test_veor3_u32(uint32x4_t a, uint32x4_t b, uint32x4_t c) {128 uint32x4_t result = veor3q_u32(a, b, c);129}130 131// CHECK-LABEL: @test_veor3_u64(132// CHECK: call <2 x i64> @llvm.aarch64.crypto.eor3u.v2i64133//134void test_veor3_u64(uint64x2_t a, uint64x2_t b, uint64x2_t c) {135 uint64x2_t result = veor3q_u64(a, b, c);136}137 138// CHECK-LABEL: @test_veor3_s8(139// CHECK: call <16 x i8> @llvm.aarch64.crypto.eor3s.v16i8140//141void test_veor3_s8(int8x16_t a, int8x16_t b, int8x16_t c) {142 int8x16_t result = veor3q_s8(a, b, c);143}144 145// CHECK-LABEL: @test_veor3_s16(146// CHECK: call <8 x i16> @llvm.aarch64.crypto.eor3s.v8i16147//148void test_veor3_s16(int16x8_t a, int16x8_t b, int16x8_t c) {149 int16x8_t result = veor3q_s16(a, b, c);150}151 152// CHECK-LABEL: @test_veor3_s32(153// CHECK: call <4 x i32> @llvm.aarch64.crypto.eor3s.v4i32154//155void test_veor3_s32(int32x4_t a, int32x4_t b, int32x4_t c) {156 int32x4_t result = veor3q_s32(a, b, c);157}158 159// CHECK-LABEL: @test_veor3_s64(160// CHECK: call <2 x i64> @llvm.aarch64.crypto.eor3s.v2i64161//162void test_veor3_s64(int64x2_t a, int64x2_t b, int64x2_t c) {163 int64x2_t result = veor3q_s64(a, b, c);164}165