| // NOTE: Assertions have been autogenerated by utils/update_cc_test_checks.py |
| // REQUIRES: aarch64-registered-target |
| // RUN: %clang_cc1 -triple aarch64 -target-feature +sve -O2 -Werror -Wall -emit-llvm -o - %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s |
| // RUN: %clang_cc1 -triple aarch64 -target-feature +sve -O2 -Werror -Wall -emit-llvm -o - -x c++ %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s -check-prefix=CPP-CHECK |
| // RUN: %clang_cc1 -fclang-abi-compat=latest -triple aarch64 -target-feature +sve -target-feature +bf16 -S -disable-O0-optnone -Werror -Wall -o /dev/null %s |
| // RUN: %clang_cc1 -fclang-abi-compat=latest -triple aarch64 -target-feature +sme -target-feature +bf16 -S -disable-O0-optnone -Werror -Wall -o /dev/null %s |
| |
| #include <arm_sve.h> |
| |
| #if defined __ARM_FEATURE_SME |
| #define MODE_ATTR __arm_streaming |
| #else |
| #define MODE_ATTR |
| #endif |
| |
| |
| // CHECK-LABEL: @test_svundef3_s8( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 16 x i8>, <vscale x 16 x i8>, <vscale x 16 x i8> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z16test_svundef3_s8v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 16 x i8>, <vscale x 16 x i8>, <vscale x 16 x i8> } undef |
| // |
| svint8x3_t test_svundef3_s8(void) MODE_ATTR |
| { |
| return svundef3_s8(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_s16( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 8 x i16>, <vscale x 8 x i16>, <vscale x 8 x i16> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z17test_svundef3_s16v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 8 x i16>, <vscale x 8 x i16>, <vscale x 8 x i16> } undef |
| // |
| svint16x3_t test_svundef3_s16(void) MODE_ATTR |
| { |
| return svundef3_s16(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_s32( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 4 x i32>, <vscale x 4 x i32>, <vscale x 4 x i32> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z17test_svundef3_s32v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 4 x i32>, <vscale x 4 x i32>, <vscale x 4 x i32> } undef |
| // |
| svint32x3_t test_svundef3_s32(void) MODE_ATTR |
| { |
| return svundef3_s32(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_s64( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 2 x i64>, <vscale x 2 x i64>, <vscale x 2 x i64> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z17test_svundef3_s64v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 2 x i64>, <vscale x 2 x i64>, <vscale x 2 x i64> } undef |
| // |
| svint64x3_t test_svundef3_s64(void) MODE_ATTR |
| { |
| return svundef3_s64(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_u8( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 16 x i8>, <vscale x 16 x i8>, <vscale x 16 x i8> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z16test_svundef3_u8v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 16 x i8>, <vscale x 16 x i8>, <vscale x 16 x i8> } undef |
| // |
| svuint8x3_t test_svundef3_u8(void) MODE_ATTR |
| { |
| return svundef3_u8(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_u16( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 8 x i16>, <vscale x 8 x i16>, <vscale x 8 x i16> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z17test_svundef3_u16v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 8 x i16>, <vscale x 8 x i16>, <vscale x 8 x i16> } undef |
| // |
| svuint16x3_t test_svundef3_u16(void) MODE_ATTR |
| { |
| return svundef3_u16(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_u32( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 4 x i32>, <vscale x 4 x i32>, <vscale x 4 x i32> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z17test_svundef3_u32v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 4 x i32>, <vscale x 4 x i32>, <vscale x 4 x i32> } undef |
| // |
| svuint32x3_t test_svundef3_u32(void) MODE_ATTR |
| { |
| return svundef3_u32(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_u64( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 2 x i64>, <vscale x 2 x i64>, <vscale x 2 x i64> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z17test_svundef3_u64v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 2 x i64>, <vscale x 2 x i64>, <vscale x 2 x i64> } undef |
| // |
| svuint64x3_t test_svundef3_u64(void) MODE_ATTR |
| { |
| return svundef3_u64(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_f16( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 8 x half>, <vscale x 8 x half>, <vscale x 8 x half> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z17test_svundef3_f16v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 8 x half>, <vscale x 8 x half>, <vscale x 8 x half> } undef |
| // |
| svfloat16x3_t test_svundef3_f16(void) MODE_ATTR |
| { |
| return svundef3_f16(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_f32( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 4 x float>, <vscale x 4 x float>, <vscale x 4 x float> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z17test_svundef3_f32v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 4 x float>, <vscale x 4 x float>, <vscale x 4 x float> } undef |
| // |
| svfloat32x3_t test_svundef3_f32(void) MODE_ATTR |
| { |
| return svundef3_f32(); |
| } |
| |
| // CHECK-LABEL: @test_svundef3_f64( |
| // CHECK-NEXT: entry: |
| // CHECK-NEXT: ret { <vscale x 2 x double>, <vscale x 2 x double>, <vscale x 2 x double> } undef |
| // |
| // CPP-CHECK-LABEL: @_Z17test_svundef3_f64v( |
| // CPP-CHECK-NEXT: entry: |
| // CPP-CHECK-NEXT: ret { <vscale x 2 x double>, <vscale x 2 x double>, <vscale x 2 x double> } undef |
| // |
| svfloat64x3_t test_svundef3_f64(void) MODE_ATTR |
| { |
| return svundef3_f64(); |
| } |