OpenE2K
/
gcc
2
0
Fork 0
Code Issues Pull Requests Projects Releases Wiki Activity
gcc/gcc/config/arm
History
Richard Earnshaw ca7e162896 [ARM] PR 82445 - suppress 32-bit aligned ldrd/strd peepholing with -mno-unaligned-access 
Peephole patterns exist in the arm backend to spot load/store
operations to adjacent memory operations in order to convert them into
ldrd/strd instructions.  However, when we have strict alignment
enforced, then we can only do this if the accesses are known to be
64-bit aligned; this is unlikely to be the case for most loads.  The
patch adds some alignment checking to the code that validates the
addresses for use in the peephole patterns.  This should also fix
incorrect generation of ldrd/strd with unaligned accesses that could
previously have occurred on ARMv5e where all such operations must be
64-bit aligned.

I've added some new tests as well.  In doing so I discovered that the
ldrd/strd peephole tests could never fail since they would match the
source file name in the scanned assembly as well as any instructions
of the intended type.  I've fixed those by tightening the scan results
slightly.

gcc:

* config/arm/arm.c (align_ok_ldrd_strd): New function.
(mem_ok_for_ldrd_strd): New parameter align.  Extract the alignment of the
mem into it.
(gen_operands_ldrd_strd): Validate the alignment of the accesses.

testsuite:

* gcc.target/arm/peep-ldrd-1.c: Tighten test scan pattern.
* gcc.target/arm/peep-strd-1.c: Likewise.
* gcc.target/arm/peep-ldrd-2.c: New test.
* gcc.target/arm/peep-strd-2.c: New test.

From-SVN: r253891
 		2017-10-19 13:14:55 +00:00
..
README-interworking Update copyright years. 2017-01-01 13:07:43 +01:00
aarch-common-protos.h Update copyright years. 2017-01-01 13:07:43 +01:00
aarch-common.c Update copyright years. 2017-01-01 13:07:43 +01:00
aarch-cost-tables.h Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
aout.h Update copyright years. 2017-01-01 13:07:43 +01:00
arm-builtins.c [ARM] Rename FPSCR builtins to correct names 2017-06-23 16:08:40 +00:00
arm-c.c Update copyright years. 2017-01-01 13:07:43 +01:00
arm-cpu-cdata.h Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
arm-cpu-data.h Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
arm-cpu.h Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
arm-cpus.in Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
arm-fixed.md Update copyright years. 2017-01-01 13:07:43 +01:00
arm-flags.h Update copyright years. 2017-01-01 13:07:43 +01:00
arm-generic.md Update copyright years. 2017-01-01 13:07:43 +01:00
arm-isa.h Fix PR80082: LDRD erronously used for 64bit load on ARMv7-R 2017-03-22 11:35:15 +00:00
arm-ldmstm.ml Update copyright years. 2017-01-01 13:07:43 +01:00
arm-modes.def Update copyright years. 2017-01-01 13:07:43 +01:00
arm-opts.h [arm] Replace command-line option .def files with single definition file 2017-01-11 14:39:00 +00:00
arm-protos.h Fix PR80082: LDRD erronously used for 64bit load on ARMv7-R 2017-03-22 11:35:15 +00:00
arm-simd-builtin-types.def Update copyright years. 2017-01-01 13:07:43 +01:00
arm-tables.opt Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
arm-tune.md Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
arm.c [ARM] PR 82445 - suppress 32-bit aligned ldrd/strd peepholing with -mno-unaligned-access 2017-10-19 13:14:55 +00:00
arm.h ARM: Introduce ARM_DEFAULT_SHORT_ENUMS 2017-04-07 07:02:07 +00:00
arm.md PR71607: Fix ICE when loading constant 2017-06-02 11:19:16 +00:00
arm.opt Update copyright years. 2017-01-01 13:07:43 +01:00
arm926ejs.md Update copyright years. 2017-01-01 13:07:43 +01:00
arm1020e.md Update copyright years. 2017-01-01 13:07:43 +01:00
arm1026ejs.md Update copyright years. 2017-01-01 13:07:43 +01:00
arm1136jfs.md Update copyright years. 2017-01-01 13:07:43 +01:00
arm_acle.h [ARM] Implement support for ACLE Coprocessor MCRR and MRRC intrinsics 2017-01-06 17:49:12 +00:00
arm_acle_builtins.def update-copyright.py: Add libhsail-rt to self.default_dirs and call self.add_dir on it. 2017-01-26 09:24:22 +01:00
arm_cmse.h Update copyright years. 2017-01-01 13:07:43 +01:00
arm_fp16.h Update copyright years. 2017-01-01 13:07:43 +01:00
arm_neon.h [ARM,AArch64] more poly64 intrinsics and tests 2017-02-10 14:18:16 +01:00
arm_neon_builtins.def Update copyright years. 2017-01-01 13:07:43 +01:00
arm_vfp_builtins.def Update copyright years. 2017-01-01 13:07:43 +01:00
bpabi.h Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
constraints.md [ARM] Implement support for ACLE Coprocessor LDC and STC intrinsics 2017-01-06 17:37:39 +00:00
cortex-a5.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a7.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a8-neon.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a8.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a9-neon.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a9.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a15-neon.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a15.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a17-neon.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a17.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-a53.md My previous change to the Cortex-A53 scheduler resulted in a 13% regression on a proprietary benchmark. 2017-01-11 16:38:42 +00:00
cortex-a57.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-m4-fpu.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-m4.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-m7.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-r4.md Update copyright years. 2017-01-01 13:07:43 +01:00
cortex-r4f.md Update copyright years. 2017-01-01 13:07:43 +01:00
crypto.def Update copyright years. 2017-01-01 13:07:43 +01:00
crypto.md Update copyright years. 2017-01-01 13:07:43 +01:00
driver-arm.c Update copyright years. 2017-01-01 13:07:43 +01:00
elf.h Update copyright years. 2017-01-01 13:07:43 +01:00
exynos-m1.md Update copyright years. 2017-01-01 13:07:43 +01:00
fa526.md Update copyright years. 2017-01-01 13:07:43 +01:00
fa606te.md Update copyright years. 2017-01-01 13:07:43 +01:00
fa626te.md Update copyright years. 2017-01-01 13:07:43 +01:00
fa726te.md Update copyright years. 2017-01-01 13:07:43 +01:00
fmp626.md Update copyright years. 2017-01-01 13:07:43 +01:00
freebsd.h Update copyright years. 2017-01-01 13:07:43 +01:00
fuchsia-elf.h fuchsia-elf.h: New file. 2017-01-10 18:00:43 +00:00
iterators.md [ARM] Implement support for ACLE Coprocessor MCRR and MRRC intrinsics 2017-01-06 17:49:12 +00:00
iwmmxt.md Update copyright years. 2017-01-01 13:07:43 +01:00
iwmmxt2.md Update copyright years. 2017-01-01 13:07:43 +01:00
ldmstm.md Update copyright years. 2017-01-01 13:07:43 +01:00
ldrdstrd.md Update copyright years. 2017-01-01 13:07:43 +01:00
linux-eabi.h Update copyright years. 2017-01-01 13:07:43 +01:00
linux-elf.h Update copyright years. 2017-01-01 13:07:43 +01:00
linux-gas.h Update copyright years. 2017-01-01 13:07:43 +01:00
marvell-f-iwmmxt.md Update copyright years. 2017-01-01 13:07:43 +01:00
marvell-pj4.md Update copyright years. 2017-01-01 13:07:43 +01:00
mmintrin.h Update copyright years. 2017-01-01 13:07:43 +01:00
neon.md [ARM] PR target/79911: Invalid vec_select arguments 2017-03-13 10:58:48 +00:00
netbsd-elf.h Update copyright years. 2017-01-01 13:07:43 +01:00
parsecpu.awk [ARM] Fix PR79742 incorrect scheduler choice. 2017-02-28 14:17:29 +00:00
predicates.md Update copyright years. 2017-01-01 13:07:43 +01:00
rtems.h [RTEMS] Add GCC Runtime Library Exception 2017-07-26 08:31:09 +00:00
semi.h Update copyright years. 2017-01-01 13:07:43 +01:00
symbian.h Update copyright years. 2017-01-01 13:07:43 +01:00
sync.md Update copyright years. 2017-01-01 13:07:43 +01:00
t-aprofile Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
t-arm [arm] Replace command-line option .def files with single definition file 2017-01-11 14:39:00 +00:00
t-arm-elf Update copyright years. 2017-01-01 13:07:43 +01:00
t-bpabi
…
t-linux-androideabi
…
t-linux-eabi Update copyright years. 2017-01-01 13:07:43 +01:00
t-phoenix Update copyright years. 2017-01-01 13:07:43 +01:00
t-rmprofile Backport patch to remove falkor aarch32 support. 2017-06-24 16:22:11 -07:00
t-rtems [RTEMS] Add vfp multilib for ARM 2016-08-24 06:05:04 +00:00
t-symbian Update copyright years. 2017-01-01 13:07:43 +01:00
t-vxworks Update copyright years. 2017-01-01 13:07:43 +01:00
thumb1.md Update copyright years. 2017-01-01 13:07:43 +01:00
thumb2.md Update copyright years. 2017-01-01 13:07:43 +01:00
types.md [ARM] Implement support for ACLE Coprocessor CDP intrinsics 2017-01-06 17:35:23 +00:00
uclinux-eabi.h Update copyright years. 2017-01-01 13:07:43 +01:00
uclinux-elf.h Update copyright years. 2017-01-01 13:07:43 +01:00
unknown-elf.h Update copyright years. 2017-01-01 13:07:43 +01:00
unspecs.md [ARM] Implement support for ACLE Coprocessor MCRR and MRRC intrinsics 2017-01-06 17:49:12 +00:00
vec-common.md Update copyright years. 2017-01-01 13:07:43 +01:00
vfp.md PR71607: Fix ICE when loading constant 2017-06-02 11:19:16 +00:00
vfp11.md Update copyright years. 2017-01-01 13:07:43 +01:00
vxworks.h Update copyright years. 2017-01-01 13:07:43 +01:00
vxworks.opt Update copyright years. 2017-01-01 13:07:43 +01:00
x-arm
…
xgene1.md Update copyright years. 2017-01-01 13:07:43 +01:00