aboutsummaryrefslogtreecommitdiff
path: root/gcc/ada/gcc-interface/ada-tree.h
diff options
context:
space:
mode:
authorWilco Dijkstra <wdijkstr@arm.com>2017-06-21 10:46:02 +0000
committerWilco Dijkstra <wilco@gcc.gnu.org>2017-06-21 10:46:02 +0000
commitdca19fe10daf00bfef714e3f9f98c63ff70c7a64 (patch)
tree299fb3d6951d77ea9481949905d0bce787c70afb /gcc/ada/gcc-interface/ada-tree.h
parentf28e54bd06f3733ff147128107a8da6d3e6d428e (diff)
downloadgcc-dca19fe10daf00bfef714e3f9f98c63ff70c7a64.zip
gcc-dca19fe10daf00bfef714e3f9f98c63ff70c7a64.tar.gz
gcc-dca19fe10daf00bfef714e3f9f98c63ff70c7a64.tar.bz2
Improve dup pattern
Improve the dup pattern to prefer vector registers. When doing a dup after a load, the register allocator thinks the costs are identical and chooses an integer load. However a dup from an integer register includes an int->fp transfer which is not modelled. Adding a '?' to the integer variant means the cost is increased slightly so we prefer using a vector register. This improves the following example: #include <arm_neon.h> void f(unsigned *a, uint32x4_t *b) { b[0] = vdupq_n_u32(a[1]); b[1] = vdupq_n_u32(a[2]); } to: ldr s0, [x0, 4] dup v0.4s, v0.s[0] str q0, [x1] ldr s0, [x0, 8] dup v0.4s, v0.s[0] str q0, [x1, 16] ret gcc/ * config/aarch64/aarch64-simd.md (aarch64_simd_dup): Swap alternatives, make integer dup more expensive. From-SVN: r249443
Diffstat (limited to 'gcc/ada/gcc-interface/ada-tree.h')
0 files changed, 0 insertions, 0 deletions