This patch supports following MVE ACLE scalar shift intrinsics. sqrshr, sqrshrl, sqrshrl_sat48, sqshl, sqshll, srshr, srshrl, uqrshl, uqrshll, uqrshll_sat48, uqshl, uqshll, urshr, urshrl, lsll, asrl. Please refer to M-profile Vector Extension (MVE) intrinsics [1] for more details. [1] https://developer.arm.com/architectures/instruction-sets/simd-isas/helium/mve-intrinsics 2020-03-23 Srinath Parvathaneni <srinath.parvathaneni@arm.com> * config/arm/arm-builtins.c (LSLL_QUALIFIERS): Define builtin qualifier. (UQSHL_QUALIFIERS): Likewise. (ASRL_QUALIFIERS): Likewise. (SQSHL_QUALIFIERS): Likewise. * config/arm/arm_mve.h (__ARM_BIG_ENDIAN): Check to not support MVE in Big-Endian Mode. (sqrshr): Define macro. (sqrshrl): Likewise. (sqrshrl_sat48): Likewise. (sqshl): Likewise. (sqshll): Likewise. (srshr): Likewise. (srshrl): Likewise. (uqrshl): Likewise. (uqrshll): Likewise. (uqrshll_sat48): Likewise. (uqshl): Likewise. (uqshll): Likewise. (urshr): Likewise. (urshrl): Likewise. (lsll): Likewise. (asrl): Likewise. (__arm_lsll): Define intrinsic. (__arm_asrl): Likewise. (__arm_uqrshll): Likewise. (__arm_uqrshll_sat48): Likewise. (__arm_sqrshrl): Likewise. (__arm_sqrshrl_sat48): Likewise. (__arm_uqshll): Likewise. (__arm_urshrl): Likewise. (__arm_srshrl): Likewise. (__arm_sqshll): Likewise. (__arm_uqrshl): Likewise. (__arm_sqrshr): Likewise. (__arm_uqshl): Likewise. (__arm_urshr): Likewise. (__arm_sqshl): Likewise. (__arm_srshr): Likewise. * config/arm/arm_mve_builtins.def (LSLL_QUALIFIERS): Use builtin qualifier. (UQSHL_QUALIFIERS): Likewise. (ASRL_QUALIFIERS): Likewise. (SQSHL_QUALIFIERS): Likewise. * config/arm/mve.md (mve_uqrshll_sat<supf>_di): Define RTL pattern. (mve_sqrshrl_sat<supf>_di): Likewise. (mve_uqrshl_si): Likewise. (mve_sqrshr_si): Likewise. (mve_uqshll_di): Likewise. (mve_urshrl_di): Likewise. (mve_uqshl_si): Likewise. (mve_urshr_si): Likewise. (mve_sqshl_si): Likewise. (mve_srshr_si): Likewise. (mve_srshrl_di): Likewise. (mve_sqshll_di): Likewise. gcc/testsuite/ChangeLog: 2020-03-23 Srinath Parvathaneni <srinath.parvathaneni@arm.com> * gcc.target/arm/mve/intrinsics/asrl.c: New test. * gcc.target/arm/mve/intrinsics/lsll.c: Likewise. * gcc.target/arm/mve/intrinsics/sqrshr.c: Likewise. * gcc.target/arm/mve/intrinsics/sqrshrl_sat48.c: Likewise. * gcc.target/arm/mve/intrinsics/sqrshrl_sat64.c: Likewise. * gcc.target/arm/mve/intrinsics/sqshl.c: Likewise. * gcc.target/arm/mve/intrinsics/sqshll.c: Likewise. * gcc.target/arm/mve/intrinsics/srshr.c: Likewise. * gcc.target/arm/mve/intrinsics/srshrl.c: Likewise. * gcc.target/arm/mve/intrinsics/uqrshl.c: Likewise. * gcc.target/arm/mve/intrinsics/uqrshll_sat48.c: Likewise. * gcc.target/arm/mve/intrinsics/uqrshll_sat64.c: Likewise. * gcc.target/arm/mve/intrinsics/uqshl.c: Likewise. * gcc.target/arm/mve/intrinsics/uqshll.c: Likewise. * gcc.target/arm/mve/intrinsics/urshr.c: Likewise. * gcc.target/arm/mve/intrinsics/urshrl.c: Likewise. * lib/target-supports.exp: (check_effective_target_arm_v8_1m_mve_fp_ok_nocache): Modify to not support MVE floating point in Big Endian mode. (check_effective_target_arm_v8_1m_mve_ok_nocache): Modify to not support MVE integer in Big Endian mode.
Name |
Last commit
|
Last update |
---|---|---|
.. | ||
README-interworking | Loading commit data... | |
aarch-common-protos.h | Loading commit data... | |
aarch-common.c | Loading commit data... | |
aarch-cost-tables.h | Loading commit data... | |
aout.h | Loading commit data... | |
arm-builtins.c | Loading commit data... | |
arm-c.c | Loading commit data... | |
arm-cpus.in | Loading commit data... | |
arm-d.c | Loading commit data... | |
arm-fixed.md | Loading commit data... | |
arm-flags.h | Loading commit data... | |
arm-generic.md | Loading commit data... | |
arm-ldmstm.ml | Loading commit data... | |
arm-modes.def | Loading commit data... | |
arm-opts.h | Loading commit data... | |
arm-protos.h | Loading commit data... | |
arm-simd-builtin-types.def | Loading commit data... | |
arm-tables.opt | Loading commit data... | |
arm-tune.md | Loading commit data... | |
arm.c | Loading commit data... | |
arm.h | Loading commit data... | |
arm.md | Loading commit data... | |
arm.opt | Loading commit data... | |
arm1020e.md | Loading commit data... | |
arm1026ejs.md | Loading commit data... | |
arm1136jfs.md | Loading commit data... | |
arm926ejs.md | Loading commit data... | |
arm_acle.h | Loading commit data... | |
arm_acle_builtins.def | Loading commit data... | |
arm_bf16.h | Loading commit data... | |
arm_cmse.h | Loading commit data... | |
arm_fp16.h | Loading commit data... | |
arm_mve.h | Loading commit data... | |
arm_mve_builtins.def | Loading commit data... | |
arm_neon.h | Loading commit data... | |
arm_neon_builtins.def | Loading commit data... | |
arm_vfp_builtins.def | Loading commit data... | |
bpabi.h | Loading commit data... | |
constraints.md | Loading commit data... | |
cortex-a15-neon.md | Loading commit data... | |
cortex-a15.md | Loading commit data... | |
cortex-a17-neon.md | Loading commit data... | |
cortex-a17.md | Loading commit data... | |
cortex-a5.md | Loading commit data... | |
cortex-a53.md | Loading commit data... | |
cortex-a57.md | Loading commit data... | |
cortex-a7.md | Loading commit data... | |
cortex-a8-neon.md | Loading commit data... | |
cortex-a8.md | Loading commit data... | |
cortex-a9-neon.md | Loading commit data... | |
cortex-a9.md | Loading commit data... | |
cortex-m4-fpu.md | Loading commit data... | |
cortex-m4.md | Loading commit data... | |
cortex-m7.md | Loading commit data... | |
cortex-r4.md | Loading commit data... | |
cortex-r4f.md | Loading commit data... | |
crypto.def | Loading commit data... | |
crypto.md | Loading commit data... | |
driver-arm.c | Loading commit data... | |
elf.h | Loading commit data... | |
exynos-m1.md | Loading commit data... | |
fa526.md | Loading commit data... | |
fa606te.md | Loading commit data... | |
fa626te.md | Loading commit data... | |
fa726te.md | Loading commit data... | |
fmp626.md | Loading commit data... | |
freebsd.h | Loading commit data... | |
fuchsia-elf.h | Loading commit data... | |
iterators.md | Loading commit data... | |
iwmmxt.md | Loading commit data... | |
iwmmxt2.md | Loading commit data... | |
ldmstm.md | Loading commit data... | |
ldrdstrd.md | Loading commit data... | |
linux-eabi.h | Loading commit data... | |
linux-elf.h | Loading commit data... | |
linux-gas.h | Loading commit data... | |
marvell-f-iwmmxt.md | Loading commit data... | |
marvell-pj4.md | Loading commit data... | |
mmintrin.h | Loading commit data... | |
mve.md | Loading commit data... | |
neon.md | Loading commit data... | |
netbsd-eabi.h | Loading commit data... | |
netbsd-elf.h | Loading commit data... | |
parsecpu.awk | Loading commit data... | |
predicates.md | Loading commit data... | |
rtems.h | Loading commit data... | |
semi.h | Loading commit data... | |
symbian.h | Loading commit data... | |
sync.md | Loading commit data... | |
t-aprofile | Loading commit data... | |
t-arm | Loading commit data... | |
t-arm-elf | Loading commit data... | |
t-bpabi | Loading commit data... | |
t-fuchsia | Loading commit data... | |
t-linux-androideabi | Loading commit data... | |
t-linux-eabi | Loading commit data... | |
t-multilib | Loading commit data... | |
t-phoenix | Loading commit data... | |
t-rmprofile | Loading commit data... | |
t-rtems | Loading commit data... | |
t-symbian | Loading commit data... | |
t-vxworks | Loading commit data... | |
thumb1.md | Loading commit data... | |
thumb2.md | Loading commit data... | |
types.md | Loading commit data... | |
uclinux-eabi.h | Loading commit data... | |
uclinux-elf.h | Loading commit data... | |
uclinuxfdpiceabi.h | Loading commit data... | |
unknown-elf.h | Loading commit data... | |
unspecs.md | Loading commit data... | |
vec-common.md | Loading commit data... | |
vfp.md | Loading commit data... | |
vfp11.md | Loading commit data... | |
vxworks.h | Loading commit data... | |
vxworks.opt | Loading commit data... | |
x-arm | Loading commit data... | |
xgene1.md | Loading commit data... |