mirror of
https://github.com/capstone-engine/llvm-capstone.git
synced 2024-12-12 01:18:53 +00:00
123064dc39
This cc1 option -fallow-half-arguments-and-returns allows __fp16 to be passed by argument and returned, without giving an error. It is currently always enabled for Arm and AArch64, by forcing the option in the driver. This means any cc1 tests (especially those needing arm_neon.h) need to specify the option too, to prevent the error from being emitted. This changes it to a target option instead, set to true for Arm and AArch64. This allows the option to be removed. Previously it was implied by -fnative_half_arguments_and_returns, which is set for certain languages like open_cl, renderscript and hlsl, so that option now too controls the errors. There were are few other non-arm uses of -fallow-half-arguments-and-returns but I believe they were unnecessary. The strictfp_builtins.c tests were converted from __fp16 to _Float16 to avoid the issues. Differential Revision: https://reviews.llvm.org/D133885
113 lines
6.3 KiB
C++
113 lines
6.3 KiB
C++
// RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -mvscale-min=4 -mvscale-max=4 -flax-vector-conversions=none -ffreestanding -fsyntax-only -verify=lax-vector-none %s
|
|
// RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -mvscale-min=4 -mvscale-max=4 -flax-vector-conversions=integer -ffreestanding -fsyntax-only -verify=lax-vector-integer %s
|
|
// RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -mvscale-min=4 -mvscale-max=4 -flax-vector-conversions=all -ffreestanding -fsyntax-only -verify=lax-vector-all %s
|
|
|
|
// REQUIRES: aarch64-registered-target || arm-registered-target
|
|
|
|
#include <arm_sve.h>
|
|
|
|
#define N __ARM_FEATURE_SVE_BITS
|
|
#define SVE_FIXED_ATTR __attribute__((arm_sve_vector_bits(N)))
|
|
#define GNU_FIXED_ATTR __attribute__((vector_size(N / 8)))
|
|
#define GNU_BOOL_FIXED_ATTR __attribute__((vector_size(N / 64)))
|
|
|
|
typedef svfloat32_t sve_fixed_float32_t SVE_FIXED_ATTR;
|
|
typedef svint32_t sve_fixed_int32_t SVE_FIXED_ATTR;
|
|
typedef svbool_t sve_fixed_bool_t SVE_FIXED_ATTR;
|
|
typedef float gnu_fixed_float32_t GNU_FIXED_ATTR;
|
|
typedef int gnu_fixed_int32_t GNU_FIXED_ATTR;
|
|
typedef int8_t gnu_fixed_bool_t GNU_BOOL_FIXED_ATTR;
|
|
|
|
void sve_allowed_with_integer_lax_conversions() {
|
|
sve_fixed_int32_t fi32;
|
|
svint64_t si64;
|
|
svbool_t sb8;
|
|
sve_fixed_bool_t fb8;
|
|
|
|
// The implicit cast here should fail if -flax-vector-conversions=none, but pass if
|
|
// -flax-vector-conversions={integer,all}.
|
|
fi32 = si64;
|
|
// lax-vector-none-error@-1 {{assigning to 'sve_fixed_int32_t' (vector of 16 'int' values) from incompatible type}}
|
|
si64 = fi32;
|
|
// lax-vector-none-error@-1 {{assigning to 'svint64_t' (aka '__SVInt64_t') from incompatible type}}
|
|
|
|
fi32 = sb8;
|
|
// lax-vector-none-error@-1 {{assigning to 'sve_fixed_int32_t' (vector of 16 'int' values) from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'sve_fixed_int32_t' (vector of 16 'int' values) from incompatible type}}
|
|
// lax-vector-all-error@-3 {{assigning to 'sve_fixed_int32_t' (vector of 16 'int' values) from incompatible type}}
|
|
sb8 = fi32;
|
|
// lax-vector-none-error@-1 {{assigning to 'svbool_t' (aka '__SVBool_t') from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'svbool_t' (aka '__SVBool_t') from incompatible type}}
|
|
// lax-vector-all-error@-3 {{assigning to 'svbool_t' (aka '__SVBool_t') from incompatible type}}
|
|
|
|
si64 = fb8;
|
|
// lax-vector-none-error@-1 {{assigning to 'svint64_t' (aka '__SVInt64_t') from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'svint64_t' (aka '__SVInt64_t') from incompatible type}}
|
|
// lax-vector-all-error@-3 {{assigning to 'svint64_t' (aka '__SVInt64_t') from incompatible type}}
|
|
|
|
fb8 = si64;
|
|
// lax-vector-none-error@-1 {{assigning to 'sve_fixed_bool_t' (vector of 8 'unsigned char' values) from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'sve_fixed_bool_t' (vector of 8 'unsigned char' values) from incompatible type}}
|
|
// lax-vector-all-error@-3 {{assigning to 'sve_fixed_bool_t' (vector of 8 'unsigned char' values) from incompatible type}}
|
|
}
|
|
|
|
void sve_allowed_with_all_lax_conversions() {
|
|
sve_fixed_float32_t ff32;
|
|
svfloat64_t sf64;
|
|
|
|
// The implicit cast here should fail if -flax-vector-conversions={none,integer}, but pass if
|
|
// -flax-vector-conversions=all.
|
|
ff32 = sf64;
|
|
// lax-vector-none-error@-1 {{assigning to 'sve_fixed_float32_t' (vector of 16 'float' values) from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'sve_fixed_float32_t' (vector of 16 'float' values) from incompatible type}}
|
|
sf64 = ff32;
|
|
// lax-vector-none-error@-1 {{assigning to 'svfloat64_t' (aka '__SVFloat64_t') from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'svfloat64_t' (aka '__SVFloat64_t') from incompatible type}}
|
|
}
|
|
|
|
void gnu_allowed_with_integer_lax_conversions() {
|
|
gnu_fixed_int32_t fi32;
|
|
svint64_t si64;
|
|
svbool_t sb8;
|
|
gnu_fixed_bool_t fb8;
|
|
|
|
// The implicit cast here should fail if -flax-vector-conversions=none, but pass if
|
|
// -flax-vector-conversions={integer,all}.
|
|
fi32 = si64;
|
|
// lax-vector-none-error@-1 {{assigning to 'gnu_fixed_int32_t' (vector of 16 'int' values) from incompatible type}}
|
|
si64 = fi32;
|
|
// lax-vector-none-error@-1 {{assigning to 'svint64_t' (aka '__SVInt64_t') from incompatible type}}
|
|
|
|
fi32 = sb8;
|
|
// lax-vector-none-error@-1 {{assigning to 'gnu_fixed_int32_t' (vector of 16 'int' values) from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'gnu_fixed_int32_t' (vector of 16 'int' values) from incompatible type}}
|
|
// lax-vector-all-error@-3 {{assigning to 'gnu_fixed_int32_t' (vector of 16 'int' values) from incompatible type}}
|
|
sb8 = fi32;
|
|
// lax-vector-none-error@-1 {{assigning to 'svbool_t' (aka '__SVBool_t') from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'svbool_t' (aka '__SVBool_t') from incompatible type}}
|
|
// lax-vector-all-error@-3 {{assigning to 'svbool_t' (aka '__SVBool_t') from incompatible type}}
|
|
|
|
fb8 = si64;
|
|
// lax-vector-none-error@-1 {{assigning to 'gnu_fixed_bool_t' (vector of 8 'int8_t' values) from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'gnu_fixed_bool_t' (vector of 8 'int8_t' values) from incompatible type}}
|
|
// lax-vector-all-error@-3 {{assigning to 'gnu_fixed_bool_t' (vector of 8 'int8_t' values) from incompatible type}}
|
|
si64 = fb8;
|
|
// lax-vector-none-error@-1 {{assigning to 'svint64_t' (aka '__SVInt64_t') from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'svint64_t' (aka '__SVInt64_t') from incompatible type}}
|
|
// lax-vector-all-error@-3 {{assigning to 'svint64_t' (aka '__SVInt64_t') from incompatible type}}
|
|
}
|
|
|
|
void gnu_allowed_with_all_lax_conversions() {
|
|
gnu_fixed_float32_t ff32;
|
|
svfloat64_t sf64;
|
|
|
|
// The implicit cast here should fail if -flax-vector-conversions={none,integer}, but pass if
|
|
// -flax-vector-conversions=all.
|
|
ff32 = sf64;
|
|
// lax-vector-none-error@-1 {{assigning to 'gnu_fixed_float32_t' (vector of 16 'float' values) from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'gnu_fixed_float32_t' (vector of 16 'float' values) from incompatible type}}
|
|
sf64 = ff32;
|
|
// lax-vector-none-error@-1 {{assigning to 'svfloat64_t' (aka '__SVFloat64_t') from incompatible type}}
|
|
// lax-vector-integer-error@-2 {{assigning to 'svfloat64_t' (aka '__SVFloat64_t') from incompatible type}}
|
|
}
|