[ARM] Remove neon_reinterpret, use casts
* config/arm/arm-protos.h (neon_reinterpret): Remove. * config/arm/arm.c (neon_reinterpret): Remove. * config/arm/arm_neon_builtins.def (vreinterpretv8qi, vreinterpretv4hi, vreinterpretv2si, vreinterpretv2sf, vreinterpretdi, vreinterpretv16qi, vreinterpretv8hi, vreinterpretv4si, vreinterpretv4sf, vreinterpretv2di, vreinterpretti): Remove. * config/arm/neon.md (neon_vreinterpretv8qi<mode>, neon_vreinterpretv4hi<mode>, neon_vreinterpretv2si<mode>, neon_vreinterpretv2sf<mode>, neon_vreinterpretdi<mode>, neon_vreinterpretti<mode>, neon_vreinterpretv16qi<mode>, neon_vreinterpretv8hi<mode>, neon_vreinterpretv4si<mode>, neon_vreinterpretv4sf<mode>, neon_vreinterpretv2di<mode>): Remove. * config/arm/arm_neon.h (vreinterpret_p8_p16, vreinterpret_p8_f32, vreinterpret_p8_p64, vreinterpret_p8_s64, vreinterpret_p8_u64, vreinterpret_p8_s8, vreinterpret_p8_s16, vreinterpret_p8_s32, vreinterpret_p8_u8, vreinterpret_p8_u16, vreinterpret_p8_u32, vreinterpret_p16_p8, vreinterpret_p16_f32, vreinterpret_p16_p64, vreinterpret_p16_s64, vreinterpret_p16_u64, vreinterpret_p16_s8, vreinterpret_p16_s16, vreinterpret_p16_s32, vreinterpret_p16_u8, vreinterpret_p16_u16, vreinterpret_p16_u32, vreinterpret_f32_p8, vreinterpret_f32_p16, vreinterpret_f32_p64, vreinterpret_f32_s64, vreinterpret_f32_u64, vreinterpret_f32_s8, vreinterpret_f32_s16, vreinterpret_f32_s32, vreinterpret_f32_u8, vreinterpret_f32_u16, vreinterpret_f32_u32, vreinterpret_p64_p8, vreinterpret_p64_p16, vreinterpret_p64_f32, vreinterpret_p64_s64, vreinterpret_p64_u64, vreinterpret_p64_s8, vreinterpret_p64_s16, vreinterpret_p64_s32, vreinterpret_p64_u8, vreinterpret_p64_u16, vreinterpret_p64_u32, vreinterpret_s64_p8, vreinterpret_s64_p16, vreinterpret_s64_f32, vreinterpret_s64_p64, vreinterpret_s64_u64, vreinterpret_s64_s8, vreinterpret_s64_s16, vreinterpret_s64_s32, vreinterpret_s64_u8, vreinterpret_s64_u16, vreinterpret_s64_u32, vreinterpret_u64_p8, vreinterpret_u64_p16, vreinterpret_u64_f32, vreinterpret_u64_p64, vreinterpret_u64_s64, vreinterpret_u64_s8, vreinterpret_u64_s16, vreinterpret_u64_s32, vreinterpret_u64_u8, vreinterpret_u64_u16, vreinterpret_u64_u32, vreinterpret_s8_p8, vreinterpret_s8_p16, vreinterpret_s8_f32, vreinterpret_s8_p64, vreinterpret_s8_s64, vreinterpret_s8_u64, vreinterpret_s8_s16, vreinterpret_s8_s32, vreinterpret_s8_u8, vreinterpret_s8_u16, vreinterpret_s8_u32, vreinterpret_s16_p8, vreinterpret_s16_p16, vreinterpret_s16_f32, vreinterpret_s16_p64, vreinterpret_s16_s64, vreinterpret_s16_u64, vreinterpret_s16_s8, vreinterpret_s16_s32, vreinterpret_s16_u8, vreinterpret_s16_u16, vreinterpret_s16_u32, vreinterpret_s32_p8, vreinterpret_s32_p16, vreinterpret_s32_f32, vreinterpret_s32_p64, vreinterpret_s32_s64, vreinterpret_s32_u64, vreinterpret_s32_s8, vreinterpret_s32_s16, vreinterpret_s32_u8, vreinterpret_s32_u16, vreinterpret_s32_u32, vreinterpret_u8_p8, vreinterpret_u8_p16, vreinterpret_u8_f32, vreinterpret_u8_p64, vreinterpret_u8_s64, vreinterpret_u8_u64, vreinterpret_u8_s8, vreinterpret_u8_s16, vreinterpret_u8_s32, vreinterpret_u8_u16, vreinterpret_u8_u32, vreinterpret_u16_p8, vreinterpret_u16_p16, vreinterpret_u16_f32, vreinterpret_u16_p64, vreinterpret_u16_s64, vreinterpret_u16_u64, vreinterpret_u16_s8, vreinterpret_u16_s16, vreinterpret_u16_s32, vreinterpret_u16_u8, vreinterpret_u16_u32, vreinterpret_u32_p8, vreinterpret_u32_p16, vreinterpret_u32_f32, vreinterpret_u32_p64, vreinterpret_u32_s64, vreinterpret_u32_u64, vreinterpret_u32_s8, vreinterpret_u32_s16, vreinterpret_u32_s32, vreinterpret_u32_u8, vreinterpret_u32_u16, vreinterpretq_p8_p16, vreinterpretq_p8_f32, vreinterpretq_p8_p64, vreinterpretq_p8_p128, vreinterpretq_p8_s64, vreinterpretq_p8_u64, vreinterpretq_p8_s8, vreinterpretq_p8_s16, vreinterpretq_p8_s32, vreinterpretq_p8_u8, vreinterpretq_p8_u16, vreinterpretq_p8_u32, vreinterpretq_p16_p8, vreinterpretq_p16_f32, vreinterpretq_p16_p64, vreinterpretq_p16_p128, vreinterpretq_p16_s64, vreinterpretq_p16_u64, vreinterpretq_p16_s8, vreinterpretq_p16_s16, vreinterpretq_p16_s32, vreinterpretq_p16_u8, vreinterpretq_p16_u16, vreinterpretq_p16_u32, vreinterpretq_f32_p8, vreinterpretq_f32_p16, vreinterpretq_f32_p64, vreinterpretq_f32_p128, vreinterpretq_f32_s64, vreinterpretq_f32_u64, vreinterpretq_f32_s8, vreinterpretq_f32_s16, vreinterpretq_f32_s32, vreinterpretq_f32_u8, vreinterpretq_f32_u16, vreinterpretq_f32_u32, vreinterpretq_p64_p8, vreinterpretq_p64_p16, vreinterpretq_p64_f32, vreinterpretq_p64_p128, vreinterpretq_p64_s64, vreinterpretq_p64_u64, vreinterpretq_p64_s8, vreinterpretq_p64_s16, vreinterpretq_p64_s32, vreinterpretq_p64_u8, vreinterpretq_p64_u16, vreinterpretq_p64_u32, vreinterpretq_p128_p8, vreinterpretq_p128_p16, vreinterpretq_p128_f32, vreinterpretq_p128_p64, vreinterpretq_p128_s64, vreinterpretq_p128_u64, vreinterpretq_p128_s8, vreinterpretq_p128_s16, vreinterpretq_p128_s32, vreinterpretq_p128_u8, vreinterpretq_p128_u16, vreinterpretq_p128_u32, vreinterpretq_s64_p8, vreinterpretq_s64_p16, vreinterpretq_s64_f32, vreinterpretq_s64_p64, vreinterpretq_s64_p128, vreinterpretq_s64_u64, vreinterpretq_s64_s8, vreinterpretq_s64_s16, vreinterpretq_s64_s32, vreinterpretq_s64_u8, vreinterpretq_s64_u16, vreinterpretq_s64_u32, vreinterpretq_u64_p8, vreinterpretq_u64_p16, vreinterpretq_u64_f32, vreinterpretq_u64_p64, vreinterpretq_u64_p128, vreinterpretq_u64_s64, vreinterpretq_u64_s8, vreinterpretq_u64_s16, vreinterpretq_u64_s32, vreinterpretq_u64_u8, vreinterpretq_u64_u16, vreinterpretq_u64_u32, vreinterpretq_s8_p8, vreinterpretq_s8_p16, vreinterpretq_s8_f32, vreinterpretq_s8_p64, vreinterpretq_s8_p128, vreinterpretq_s8_s64, vreinterpretq_s8_u64, vreinterpretq_s8_s16, vreinterpretq_s8_s32, vreinterpretq_s8_u8, vreinterpretq_s8_u16, vreinterpretq_s8_u32, vreinterpretq_s16_p8, vreinterpretq_s16_p16, vreinterpretq_s16_f32, vreinterpretq_s16_p64, vreinterpretq_s16_p128, vreinterpretq_s16_s64, vreinterpretq_s16_u64, vreinterpretq_s16_s8, vreinterpretq_s16_s32, vreinterpretq_s16_u8, vreinterpretq_s16_u16, vreinterpretq_s16_u32, vreinterpretq_s32_p8, vreinterpretq_s32_p16, vreinterpretq_s32_f16, vreinterpretq_s32_f32, vreinterpretq_s32_p64, vreinterpretq_s32_p128, vreinterpretq_s32_s64, vreinterpretq_s32_u64, vreinterpretq_s32_s8, vreinterpretq_s32_s16, vreinterpretq_s32_u8, vreinterpretq_s32_u16, vreinterpretq_s32_u32, vreinterpretq_u8_p8, vreinterpretq_u8_p16, vreinterpretq_u8_f32, vreinterpretq_u8_p64, vreinterpretq_u8_p128, vreinterpretq_u8_s64, vreinterpretq_u8_u64, vreinterpretq_u8_s8, vreinterpretq_u8_s16, vreinterpretq_u8_s32, vreinterpretq_u8_u16, vreinterpretq_u8_u32, vreinterpretq_u16_p8, vreinterpretq_u16_p16, vreinterpretq_u16_f32, vreinterpretq_u16_p64, vreinterpretq_u16_p128, vreinterpretq_u16_s64, vreinterpretq_u16_u64, vreinterpretq_u16_s8, vreinterpretq_u16_s16, vreinterpretq_u16_s32, vreinterpretq_u16_u8, vreinterpretq_u16_u32, vreinterpretq_u32_p8, vreinterpretq_u32_p16, vreinterpretq_u32_f32, vreinterpretq_u32_p64, vreinterpretq_u32_p128, vreinterpretq_u32_s64, vreinterpretq_u32_u64, vreinterpretq_u32_s8, vreinterpretq_u32_s16, vreinterpretq_u32_s32, vreinterpretq_u32_u8, vreinterpretq_u32_u16): Rewrite using casts. From-SVN: r233142
This commit is contained in:
Alan Lawrence
Alan Lawrence
parent
d44cb386b8
commit
1d10863481
6 changed files with 401 additions and 408 deletions
112
gcc/ChangeLog
112
gcc/ChangeLog
|
|
@ -1,3 +1,115 @@
|
|||
2016-02-04 Alan Lawrence <alan.lawrence@arm.com>
|
||||
|
||||
* config/arm/arm-protos.h (neon_reinterpret): Remove.
|
||||
* config/arm/arm.c (neon_reinterpret): Remove.
|
||||
* config/arm/arm_neon_builtins.def (vreinterpretv8qi, vreinterpretv4hi,
|
||||
vreinterpretv2si, vreinterpretv2sf, vreinterpretdi, vreinterpretv16qi,
|
||||
vreinterpretv8hi, vreinterpretv4si, vreinterpretv4sf, vreinterpretv2di,
|
||||
vreinterpretti): Remove.
|
||||
* config/arm/neon.md (neon_vreinterpretv8qi<mode>,
|
||||
neon_vreinterpretv4hi<mode>, neon_vreinterpretv2si<mode>,
|
||||
neon_vreinterpretv2sf<mode>, neon_vreinterpretdi<mode>,
|
||||
neon_vreinterpretti<mode>, neon_vreinterpretv16qi<mode>,
|
||||
neon_vreinterpretv8hi<mode>, neon_vreinterpretv4si<mode>,
|
||||
neon_vreinterpretv4sf<mode>, neon_vreinterpretv2di<mode>): Remove.
|
||||
* config/arm/arm_neon.h (vreinterpret_p8_p16, vreinterpret_p8_f32,
|
||||
vreinterpret_p8_p64, vreinterpret_p8_s64, vreinterpret_p8_u64,
|
||||
vreinterpret_p8_s8, vreinterpret_p8_s16, vreinterpret_p8_s32,
|
||||
vreinterpret_p8_u8, vreinterpret_p8_u16, vreinterpret_p8_u32,
|
||||
vreinterpret_p16_p8, vreinterpret_p16_f32, vreinterpret_p16_p64,
|
||||
vreinterpret_p16_s64, vreinterpret_p16_u64, vreinterpret_p16_s8,
|
||||
vreinterpret_p16_s16, vreinterpret_p16_s32, vreinterpret_p16_u8,
|
||||
vreinterpret_p16_u16, vreinterpret_p16_u32, vreinterpret_f32_p8,
|
||||
vreinterpret_f32_p16, vreinterpret_f32_p64, vreinterpret_f32_s64,
|
||||
vreinterpret_f32_u64, vreinterpret_f32_s8, vreinterpret_f32_s16,
|
||||
vreinterpret_f32_s32, vreinterpret_f32_u8, vreinterpret_f32_u16,
|
||||
vreinterpret_f32_u32, vreinterpret_p64_p8, vreinterpret_p64_p16,
|
||||
vreinterpret_p64_f32, vreinterpret_p64_s64, vreinterpret_p64_u64,
|
||||
vreinterpret_p64_s8, vreinterpret_p64_s16, vreinterpret_p64_s32,
|
||||
vreinterpret_p64_u8, vreinterpret_p64_u16, vreinterpret_p64_u32,
|
||||
vreinterpret_s64_p8, vreinterpret_s64_p16, vreinterpret_s64_f32,
|
||||
vreinterpret_s64_p64, vreinterpret_s64_u64, vreinterpret_s64_s8,
|
||||
vreinterpret_s64_s16, vreinterpret_s64_s32, vreinterpret_s64_u8,
|
||||
vreinterpret_s64_u16, vreinterpret_s64_u32, vreinterpret_u64_p8,
|
||||
vreinterpret_u64_p16, vreinterpret_u64_f32, vreinterpret_u64_p64,
|
||||
vreinterpret_u64_s64, vreinterpret_u64_s8, vreinterpret_u64_s16,
|
||||
vreinterpret_u64_s32, vreinterpret_u64_u8, vreinterpret_u64_u16,
|
||||
vreinterpret_u64_u32, vreinterpret_s8_p8, vreinterpret_s8_p16,
|
||||
vreinterpret_s8_f32, vreinterpret_s8_p64, vreinterpret_s8_s64,
|
||||
vreinterpret_s8_u64, vreinterpret_s8_s16, vreinterpret_s8_s32,
|
||||
vreinterpret_s8_u8, vreinterpret_s8_u16, vreinterpret_s8_u32,
|
||||
vreinterpret_s16_p8, vreinterpret_s16_p16, vreinterpret_s16_f32,
|
||||
vreinterpret_s16_p64, vreinterpret_s16_s64, vreinterpret_s16_u64,
|
||||
vreinterpret_s16_s8, vreinterpret_s16_s32, vreinterpret_s16_u8,
|
||||
vreinterpret_s16_u16, vreinterpret_s16_u32, vreinterpret_s32_p8,
|
||||
vreinterpret_s32_p16, vreinterpret_s32_f32, vreinterpret_s32_p64,
|
||||
vreinterpret_s32_s64, vreinterpret_s32_u64, vreinterpret_s32_s8,
|
||||
vreinterpret_s32_s16, vreinterpret_s32_u8, vreinterpret_s32_u16,
|
||||
vreinterpret_s32_u32, vreinterpret_u8_p8, vreinterpret_u8_p16,
|
||||
vreinterpret_u8_f32, vreinterpret_u8_p64, vreinterpret_u8_s64,
|
||||
vreinterpret_u8_u64, vreinterpret_u8_s8, vreinterpret_u8_s16,
|
||||
vreinterpret_u8_s32, vreinterpret_u8_u16, vreinterpret_u8_u32,
|
||||
vreinterpret_u16_p8, vreinterpret_u16_p16, vreinterpret_u16_f32,
|
||||
vreinterpret_u16_p64, vreinterpret_u16_s64, vreinterpret_u16_u64,
|
||||
vreinterpret_u16_s8, vreinterpret_u16_s16, vreinterpret_u16_s32,
|
||||
vreinterpret_u16_u8, vreinterpret_u16_u32, vreinterpret_u32_p8,
|
||||
vreinterpret_u32_p16, vreinterpret_u32_f32, vreinterpret_u32_p64,
|
||||
vreinterpret_u32_s64, vreinterpret_u32_u64, vreinterpret_u32_s8,
|
||||
vreinterpret_u32_s16, vreinterpret_u32_s32, vreinterpret_u32_u8,
|
||||
vreinterpret_u32_u16, vreinterpretq_p8_p16, vreinterpretq_p8_f32,
|
||||
vreinterpretq_p8_p64, vreinterpretq_p8_p128, vreinterpretq_p8_s64,
|
||||
vreinterpretq_p8_u64, vreinterpretq_p8_s8, vreinterpretq_p8_s16,
|
||||
vreinterpretq_p8_s32, vreinterpretq_p8_u8, vreinterpretq_p8_u16,
|
||||
vreinterpretq_p8_u32, vreinterpretq_p16_p8, vreinterpretq_p16_f32,
|
||||
vreinterpretq_p16_p64, vreinterpretq_p16_p128, vreinterpretq_p16_s64,
|
||||
vreinterpretq_p16_u64, vreinterpretq_p16_s8, vreinterpretq_p16_s16,
|
||||
vreinterpretq_p16_s32, vreinterpretq_p16_u8, vreinterpretq_p16_u16,
|
||||
vreinterpretq_p16_u32, vreinterpretq_f32_p8, vreinterpretq_f32_p16,
|
||||
vreinterpretq_f32_p64, vreinterpretq_f32_p128, vreinterpretq_f32_s64,
|
||||
vreinterpretq_f32_u64, vreinterpretq_f32_s8, vreinterpretq_f32_s16,
|
||||
vreinterpretq_f32_s32, vreinterpretq_f32_u8, vreinterpretq_f32_u16,
|
||||
vreinterpretq_f32_u32, vreinterpretq_p64_p8, vreinterpretq_p64_p16,
|
||||
vreinterpretq_p64_f32, vreinterpretq_p64_p128, vreinterpretq_p64_s64,
|
||||
vreinterpretq_p64_u64, vreinterpretq_p64_s8, vreinterpretq_p64_s16,
|
||||
vreinterpretq_p64_s32, vreinterpretq_p64_u8, vreinterpretq_p64_u16,
|
||||
vreinterpretq_p64_u32, vreinterpretq_p128_p8, vreinterpretq_p128_p16,
|
||||
vreinterpretq_p128_f32, vreinterpretq_p128_p64, vreinterpretq_p128_s64,
|
||||
vreinterpretq_p128_u64, vreinterpretq_p128_s8, vreinterpretq_p128_s16,
|
||||
vreinterpretq_p128_s32, vreinterpretq_p128_u8, vreinterpretq_p128_u16,
|
||||
vreinterpretq_p128_u32, vreinterpretq_s64_p8, vreinterpretq_s64_p16,
|
||||
vreinterpretq_s64_f32, vreinterpretq_s64_p64, vreinterpretq_s64_p128,
|
||||
vreinterpretq_s64_u64, vreinterpretq_s64_s8, vreinterpretq_s64_s16,
|
||||
vreinterpretq_s64_s32, vreinterpretq_s64_u8, vreinterpretq_s64_u16,
|
||||
vreinterpretq_s64_u32, vreinterpretq_u64_p8, vreinterpretq_u64_p16,
|
||||
vreinterpretq_u64_f32, vreinterpretq_u64_p64, vreinterpretq_u64_p128,
|
||||
vreinterpretq_u64_s64, vreinterpretq_u64_s8, vreinterpretq_u64_s16,
|
||||
vreinterpretq_u64_s32, vreinterpretq_u64_u8, vreinterpretq_u64_u16,
|
||||
vreinterpretq_u64_u32, vreinterpretq_s8_p8, vreinterpretq_s8_p16,
|
||||
vreinterpretq_s8_f32, vreinterpretq_s8_p64, vreinterpretq_s8_p128,
|
||||
vreinterpretq_s8_s64, vreinterpretq_s8_u64, vreinterpretq_s8_s16,
|
||||
vreinterpretq_s8_s32, vreinterpretq_s8_u8, vreinterpretq_s8_u16,
|
||||
vreinterpretq_s8_u32, vreinterpretq_s16_p8, vreinterpretq_s16_p16,
|
||||
vreinterpretq_s16_f32, vreinterpretq_s16_p64, vreinterpretq_s16_p128,
|
||||
vreinterpretq_s16_s64, vreinterpretq_s16_u64, vreinterpretq_s16_s8,
|
||||
vreinterpretq_s16_s32, vreinterpretq_s16_u8, vreinterpretq_s16_u16,
|
||||
vreinterpretq_s16_u32, vreinterpretq_s32_p8, vreinterpretq_s32_p16,
|
||||
vreinterpretq_s32_f16, vreinterpretq_s32_f32, vreinterpretq_s32_p64,
|
||||
vreinterpretq_s32_p128, vreinterpretq_s32_s64, vreinterpretq_s32_u64,
|
||||
vreinterpretq_s32_s8, vreinterpretq_s32_s16, vreinterpretq_s32_u8,
|
||||
vreinterpretq_s32_u16, vreinterpretq_s32_u32, vreinterpretq_u8_p8,
|
||||
vreinterpretq_u8_p16, vreinterpretq_u8_f32, vreinterpretq_u8_p64,
|
||||
vreinterpretq_u8_p128, vreinterpretq_u8_s64, vreinterpretq_u8_u64,
|
||||
vreinterpretq_u8_s8, vreinterpretq_u8_s16, vreinterpretq_u8_s32,
|
||||
vreinterpretq_u8_u16, vreinterpretq_u8_u32, vreinterpretq_u16_p8,
|
||||
vreinterpretq_u16_p16, vreinterpretq_u16_f32, vreinterpretq_u16_p64,
|
||||
vreinterpretq_u16_p128, vreinterpretq_u16_s64, vreinterpretq_u16_u64,
|
||||
vreinterpretq_u16_s8, vreinterpretq_u16_s16, vreinterpretq_u16_s32,
|
||||
vreinterpretq_u16_u8, vreinterpretq_u16_u32, vreinterpretq_u32_p8,
|
||||
vreinterpretq_u32_p16, vreinterpretq_u32_f32, vreinterpretq_u32_p64,
|
||||
vreinterpretq_u32_p128, vreinterpretq_u32_s64, vreinterpretq_u32_u64,
|
||||
vreinterpretq_u32_s8, vreinterpretq_u32_s16, vreinterpretq_u32_s32,
|
||||
vreinterpretq_u32_u8, vreinterpretq_u32_u16): Rewrite using casts.
|
||||
|
||||
2016-02-04 Martin Liska <mliska@suse.cz>
|
||||
|
||||
PR sanitizer/69276
|
||||
|
|
|
|||
|
|
@ -89,7 +89,6 @@ extern void neon_expand_vector_init (rtx, rtx);
|
|||
extern void neon_lane_bounds (rtx, HOST_WIDE_INT, HOST_WIDE_INT, const_tree);
|
||||
extern void neon_const_bounds (rtx, HOST_WIDE_INT, HOST_WIDE_INT);
|
||||
extern HOST_WIDE_INT neon_element_bits (machine_mode);
|
||||
extern void neon_reinterpret (rtx, rtx);
|
||||
extern void neon_emit_pair_result_insn (machine_mode,
|
||||
rtx (*) (rtx, rtx, rtx, rtx),
|
||||
rtx, rtx, rtx);
|
||||
|
|
|
|||
|
|
@ -23605,13 +23605,6 @@ arm_scalar_mode_supported_p (machine_mode mode)
|
|||
return default_scalar_mode_supported_p (mode);
|
||||
}
|
||||
|
||||
/* Emit code to reinterpret one Neon type as another, without altering bits. */
|
||||
void
|
||||
neon_reinterpret (rtx dest, rtx src)
|
||||
{
|
||||
emit_move_insn (dest, gen_lowpart (GET_MODE (dest), src));
|
||||
}
|
||||
|
||||
/* Set up OPERANDS for a register copy from SRC to DEST, taking care
|
||||
not to early-clobber SRC registers in the process.
|
||||
|
||||
|
|
|
|||
File diff suppressed because it is too large
Load diff
|
|
@ -235,17 +235,6 @@ VAR1 (TERNOP, vtbx1, v8qi)
|
|||
VAR1 (TERNOP, vtbx2, v8qi)
|
||||
VAR1 (TERNOP, vtbx3, v8qi)
|
||||
VAR1 (TERNOP, vtbx4, v8qi)
|
||||
VAR5 (UNOP, vreinterpretv8qi, v8qi, v4hi, v2si, v2sf, di)
|
||||
VAR5 (UNOP, vreinterpretv4hi, v8qi, v4hi, v2si, v2sf, di)
|
||||
VAR5 (UNOP, vreinterpretv2si, v8qi, v4hi, v2si, v2sf, di)
|
||||
VAR5 (UNOP, vreinterpretv2sf, v8qi, v4hi, v2si, v2sf, di)
|
||||
VAR5 (UNOP, vreinterpretdi, v8qi, v4hi, v2si, v2sf, di)
|
||||
VAR6 (UNOP, vreinterpretv16qi, v16qi, v8hi, v4si, v4sf, v2di, ti)
|
||||
VAR6 (UNOP, vreinterpretv8hi, v16qi, v8hi, v4si, v4sf, v2di, ti)
|
||||
VAR6 (UNOP, vreinterpretv4si, v16qi, v8hi, v4si, v4sf, v2di, ti)
|
||||
VAR6 (UNOP, vreinterpretv4sf, v16qi, v8hi, v4si, v4sf, v2di, ti)
|
||||
VAR6 (UNOP, vreinterpretv2di, v16qi, v8hi, v4si, v4sf, v2di, ti)
|
||||
VAR6 (UNOP, vreinterpretti, v16qi, v8hi, v4si, v4sf, v2di, ti)
|
||||
VAR12 (LOAD1, vld1,
|
||||
v8qi, v4hi, v4hf, v2si, v2sf, di, v16qi, v8hi, v8hf, v4si, v4sf, v2di)
|
||||
VAR10 (LOAD1LANE, vld1_lane,
|
||||
|
|
|
|||
|
|
@ -4240,106 +4240,6 @@ if (BYTES_BIG_ENDIAN)
|
|||
[(set_attr "type" "neon_zip<q>")]
|
||||
)
|
||||
|
||||
(define_expand "neon_vreinterpretv8qi<mode>"
|
||||
[(match_operand:V8QI 0 "s_register_operand" "")
|
||||
(match_operand:VD_RE 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "neon_vreinterpretv4hi<mode>"
|
||||
[(match_operand:V4HI 0 "s_register_operand" "")
|
||||
(match_operand:VD_RE 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "neon_vreinterpretv2si<mode>"
|
||||
[(match_operand:V2SI 0 "s_register_operand" "")
|
||||
(match_operand:VD_RE 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "neon_vreinterpretv2sf<mode>"
|
||||
[(match_operand:V2SF 0 "s_register_operand" "")
|
||||
(match_operand:VD_RE 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "neon_vreinterpretdi<mode>"
|
||||
[(match_operand:DI 0 "s_register_operand" "")
|
||||
(match_operand:VD_RE 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "neon_vreinterpretti<mode>"
|
||||
[(match_operand:TI 0 "s_register_operand" "")
|
||||
(match_operand:VQXMOV 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
|
||||
(define_expand "neon_vreinterpretv16qi<mode>"
|
||||
[(match_operand:V16QI 0 "s_register_operand" "")
|
||||
(match_operand:VQXMOV 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "neon_vreinterpretv8hi<mode>"
|
||||
[(match_operand:V8HI 0 "s_register_operand" "")
|
||||
(match_operand:VQXMOV 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "neon_vreinterpretv4si<mode>"
|
||||
[(match_operand:V4SI 0 "s_register_operand" "")
|
||||
(match_operand:VQXMOV 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "neon_vreinterpretv4sf<mode>"
|
||||
[(match_operand:V4SF 0 "s_register_operand" "")
|
||||
(match_operand:VQXMOV 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "neon_vreinterpretv2di<mode>"
|
||||
[(match_operand:V2DI 0 "s_register_operand" "")
|
||||
(match_operand:VQXMOV 1 "s_register_operand" "")]
|
||||
"TARGET_NEON"
|
||||
{
|
||||
neon_reinterpret (operands[0], operands[1]);
|
||||
DONE;
|
||||
})
|
||||
|
||||
(define_expand "vec_load_lanes<mode><mode>"
|
||||
[(set (match_operand:VDQX 0 "s_register_operand")
|
||||
(unspec:VDQX [(match_operand:VDQX 1 "neon_struct_operand")]
|
||||
|
|
|
|||
Loading…
Add table
Reference in a new issue