// 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_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z14test_svset4_s810svint8x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svint8x4_t test_svset4_s8(svint8x4_t tuple, svint8_t x) ATTR { return SVE_ACLE_FUNC(svset4,_s8,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_s1611svint16x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svint16x4_t test_svset4_s16(svint16x4_t tuple, svint16_t x) ATTR { return SVE_ACLE_FUNC(svset4,_s16,,)(tuple, 3, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_s3211svint32x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svint32x4_t test_svset4_s32(svint32x4_t tuple, svint32_t x) ATTR { return SVE_ACLE_FUNC(svset4,_s32,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_s6411svint64x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svint64x4_t test_svset4_s64(svint64x4_t tuple, svint64_t x) ATTR { return SVE_ACLE_FUNC(svset4,_s64,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z14test_svset4_u811svuint8x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svuint8x4_t test_svset4_u8(svuint8x4_t tuple, svuint8_t x) ATTR { return SVE_ACLE_FUNC(svset4,_u8,,)(tuple, 3, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_u1612svuint16x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svuint16x4_t test_svset4_u16(svuint16x4_t tuple, svuint16_t x) ATTR { return SVE_ACLE_FUNC(svset4,_u16,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_u3212svuint32x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svuint32x4_t test_svset4_u32(svuint32x4_t tuple, svuint32_t x) ATTR { return SVE_ACLE_FUNC(svset4,_u32,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_u6412svuint64x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svuint64x4_t test_svset4_u64(svuint64x4_t tuple, svuint64_t x) ATTR { return SVE_ACLE_FUNC(svset4,_u64,,)(tuple, 3, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_f1613svfloat16x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svfloat16x4_t test_svset4_f16(svfloat16x4_t tuple, svfloat16_t x) ATTR { return SVE_ACLE_FUNC(svset4,_f16,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_f3213svfloat32x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svfloat32x4_t test_svset4_f32(svfloat32x4_t tuple, svfloat32_t x) ATTR { return SVE_ACLE_FUNC(svset4,_f32,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_f6413svfloat64x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svfloat64x4_t test_svset4_f64(svfloat64x4_t tuple, svfloat64_t x) ATTR { return SVE_ACLE_FUNC(svset4,_f64,,)(tuple, 3, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z15test_svset4_mf813svmfloat8x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svmfloat8x4_t test_svset4_mf8(svmfloat8x4_t tuple, svmfloat8_t x) ATTR { return SVE_ACLE_FUNC(svset4,_mf8,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 0 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z18test_svset4_bf16_014svbfloat16x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 0 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svbfloat16x4_t test_svset4_bf16_0(svbfloat16x4_t tuple, svbfloat16_t x) ATTR { return SVE_ACLE_FUNC(svset4,_bf16,,)(tuple, 0, x); } // CHECK-LABEL: @test_svset4_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]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z18test_svset4_bf16_114svbfloat16x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 1 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svbfloat16x4_t test_svset4_bf16_1(svbfloat16x4_t tuple, svbfloat16_t x) ATTR { return SVE_ACLE_FUNC(svset4,_bf16,,)(tuple, 1, x); } // CHECK-LABEL: @test_svset4_bf16_2( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , , , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , , , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , , , } [[TMP1]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 2 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z18test_svset4_bf16_214svbfloat16x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 2 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svbfloat16x4_t test_svset4_bf16_2(svbfloat16x4_t tuple, svbfloat16_t x) ATTR { return SVE_ACLE_FUNC(svset4,_bf16,,)(tuple, 2, x); } // CHECK-LABEL: @test_svset4_bf16_3( // CHECK-NEXT: entry: // CHECK-NEXT: [[TMP0:%.*]] = insertvalue { , , , } poison, [[TUPLE_COERCE0:%.*]], 0 // CHECK-NEXT: [[TMP1:%.*]] = insertvalue { , , , } [[TMP0]], [[TUPLE_COERCE1:%.*]], 1 // CHECK-NEXT: [[TMP2:%.*]] = insertvalue { , , , } [[TMP1]], [[TUPLE_COERCE2:%.*]], 2 // CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CHECK-NEXT: ret { , , , } [[TMP4]] // // CPP-CHECK-LABEL: @_Z18test_svset4_bf16_314svbfloat16x4_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]], [[TUPLE_COERCE2:%.*]], 2 // CPP-CHECK-NEXT: [[TMP3:%.*]] = insertvalue { , , , } [[TMP2]], [[TUPLE_COERCE3:%.*]], 3 // CPP-CHECK-NEXT: [[TMP4:%.*]] = insertvalue { , , , } [[TMP3]], [[X:%.*]], 3 // CPP-CHECK-NEXT: ret { , , , } [[TMP4]] // svbfloat16x4_t test_svset4_bf16_3(svbfloat16x4_t tuple, svbfloat16_t x) ATTR { return SVE_ACLE_FUNC(svset4,_bf16,,)(tuple, 3, x); }