// NOTE: Assertions have been autogenerated by utils/update_cc_test_checks.py // REQUIRES: aarch64-registered-target // RUN: %clang_cc1 -triple aarch64 -target-feature +sve -disable-O0-optnone -Werror -Wall -emit-llvm -o - %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s // RUN: %clang_cc1 -triple aarch64 -target-feature +sve -disable-O0-optnone -Werror -Wall -emit-llvm -o - -x c++ %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s -check-prefix=CPP-CHECK // RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64 -target-feature +sve -disable-O0-optnone -Werror -Wall -emit-llvm -o - %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s // RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64 -target-feature +sve -disable-O0-optnone -Werror -Wall -emit-llvm -o - -x c++ %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s -check-prefix=CPP-CHECK // RUN: %clang_cc1 -triple aarch64 -target-feature +sve -target-feature +sme -S -disable-O0-optnone -Werror -Wall -o /dev/null %s // RUN: %clang_cc1 -triple aarch64 -target-feature +sme -S -disable-O0-optnone -Werror -Wall -o /dev/null %s #include #ifdef SVE_OVERLOADED_FORMS // A simple used,unused... macro, long enough to represent any SVE builtin. #define SVE_ACLE_FUNC(A1,A2_UNUSED,A3,A4_UNUSED) A1##A3 #else #define SVE_ACLE_FUNC(A1,A2,A3,A4) A1##A2##A3##A4 #endif #ifdef __ARM_FEATURE_SME #define ATTR __arm_streaming #else #define ATTR #endif // CHECK-LABEL: @test_svset2_s8( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z14test_svset2_s810svint8x2_tu10__SVInt8_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svint8x2_t test_svset2_s8(svint8x2_t tuple, svint8_t x) ATTR { return SVE_ACLE_FUNC(svset2,_s8,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset2_s16( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_s1611svint16x2_tu11__SVInt16_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svint16x2_t test_svset2_s16(svint16x2_t tuple, svint16_t x) ATTR { return SVE_ACLE_FUNC(svset2,_s16,,)(tuple, 0, x); } // CHECK-LABEL: @test_svset2_s32( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_s3211svint32x2_tu11__SVInt32_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svint32x2_t test_svset2_s32(svint32x2_t tuple, svint32_t x) ATTR { return SVE_ACLE_FUNC(svset2,_s32,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset2_s64( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_s6411svint64x2_tu11__SVInt64_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svint64x2_t test_svset2_s64(svint64x2_t tuple, svint64_t x) ATTR { return SVE_ACLE_FUNC(svset2,_s64,,)(tuple, 0, x); } // CHECK-LABEL: @test_svset2_u8( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z14test_svset2_u811svuint8x2_tu11__SVUint8_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svuint8x2_t test_svset2_u8(svuint8x2_t tuple, svuint8_t x) ATTR { return SVE_ACLE_FUNC(svset2,_u8,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset2_u16( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_u1612svuint16x2_tu12__SVUint16_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svuint16x2_t test_svset2_u16(svuint16x2_t tuple, svuint16_t x) ATTR { return SVE_ACLE_FUNC(svset2,_u16,,)(tuple, 0, x); } // CHECK-LABEL: @test_svset2_u32( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_u3212svuint32x2_tu12__SVUint32_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svuint32x2_t test_svset2_u32(svuint32x2_t tuple, svuint32_t x) ATTR { return SVE_ACLE_FUNC(svset2,_u32,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset2_u64( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_u6412svuint64x2_tu12__SVUint64_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svuint64x2_t test_svset2_u64(svuint64x2_t tuple, svuint64_t x) ATTR { return SVE_ACLE_FUNC(svset2,_u64,,)(tuple, 0, x); } // CHECK-LABEL: @test_svset2_f16( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_f1613svfloat16x2_tu13__SVFloat16_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svfloat16x2_t test_svset2_f16(svfloat16x2_t tuple, svfloat16_t x) ATTR { return SVE_ACLE_FUNC(svset2,_f16,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset2_f32( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_f3213svfloat32x2_tu13__SVFloat32_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svfloat32x2_t test_svset2_f32(svfloat32x2_t tuple, svfloat32_t x) ATTR { return SVE_ACLE_FUNC(svset2,_f32,,)(tuple, 0, x); } // CHECK-LABEL: @test_svset2_f64( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_f6413svfloat64x2_tu13__SVFloat64_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svfloat64x2_t test_svset2_f64(svfloat64x2_t tuple, svfloat64_t x) ATTR { return SVE_ACLE_FUNC(svset2,_f64,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset2_mf8( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z15test_svset2_mf813svmfloat8x2_tu13__SVMfloat8_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svmfloat8x2_t test_svset2_mf8(svmfloat8x2_t tuple, svmfloat8_t x) ATTR { return SVE_ACLE_FUNC(svset2,_mf8,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset2_bf16_0( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z18test_svset2_bf16_014svbfloat16x2_tu14__SVBfloat16_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 0 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svbfloat16x2_t test_svset2_bf16_0(svbfloat16x2_t tuple, svbfloat16_t x) ATTR { return SVE_ACLE_FUNC(svset2,_bf16,,)(tuple, 0, x); } // CHECK-LABEL: @test_svset2_bf16_1( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CHECK-NEXT: ret { , } [[TMP2]] // // CPP-CHECK-LABEL: @_Z18test_svset2_bf16_114svbfloat16x2_tu14__SVBfloat16_t( // CPP-CHECK-NEXT: entry: // CPP-CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , } poison, [[TUPLE_COERCE0:%.*]], 0 // CPP-CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CPP-CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , } [[TMP1]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , } [[TMP2]] // svbfloat16x2_t test_svset2_bf16_1(svbfloat16x2_t tuple, svbfloat16_t x) ATTR { return SVE_ACLE_FUNC(svset2,_bf16,,)(tuple, 1, x); }