diff options
author | Wilco Dijkstra <wdijkstr@arm.com> | 2017-06-21 10:46:02 +0000 |
---|---|---|
committer | Wilco Dijkstra <wilco@gcc.gnu.org> | 2017-06-21 10:46:02 +0000 |
commit | dca19fe10daf00bfef714e3f9f98c63ff70c7a64 (patch) | |
tree | 299fb3d6951d77ea9481949905d0bce787c70afb /gcc/ada/gcc-interface/ada-tree.h | |
parent | f28e54bd06f3733ff147128107a8da6d3e6d428e (diff) | |
download | gcc-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