[Bug target/72758] New: GCC 4.9.2 on Aarch64 missing vreinterpretq_u64_p128 and friends

["noloader at gmail dot com" <gcc-bugzilla at gcc dot gnu dot org>]

https://gcc.gnu.org/bugzilla/show_bug.cgi?id=72758

            Bug ID: 72758
           Summary: GCC 4.9.2 on Aarch64 missing vreinterpretq_u64_p128
                    and friends
           Product: gcc
           Version: 4.9.2
            Status: UNCONFIRMED
          Severity: normal
          Priority: P3
         Component: target
          Assignee: unassigned at gcc dot gnu.org
          Reporter: noloader at gmail dot com
  Target Milestone: ---

Created attachment 39035
  --> https://gcc.gnu.org/bugzilla/attachment.cgi?id=39035&action=edit
Preprocessed test.cc

I'm working on a HiKey, which is Aarch64. The machine is powered by Linaro, and
it uses GCC 4.9.2 toolchain.

I'm using vmull_p64 and vmull_p642. I'm having trouble finding
vreinterpretq_u64_p128 (and friends) to help convert the polynomial. The
minimal test case is:

$ cat test.cc
#include <arm_neon.h>
#include <arm_acle.h>
int main(int argc, char* argv[])
{
  poly64_t a = {0};
  uint64x2_t b = vreinterpretq_u64_p128(a);
  return 0;
}

$ gcc -march=armv8-a+crc+crypto -mtune=cortex-a53 test.cc -o test.exe
test.cc: In function ‘int main(int, char**)’:
test.cc:6:42: error: ‘vreinterpretq_u64_p128’ was not declared in this scope
   uint64x2_t b = vreinterpretq_u64_p128(a);
                                          ^
*****

vreinterpretq_u64_p128 can't be found in arm_neon.h or arm_acle.h on the Linaro
machine:

$ grep p128 /usr/lib/gcc/aarch64-linux-gnu/4.9/include/arm_acle.h
$ grep p128 /usr/lib/gcc/aarch64-linux-gnu/4.9/include/arm_neon.h
$ grep p64 /usr/lib/gcc/aarch64-linux-gnu/4.9/include/arm_acle.h
$ grep p64 /usr/lib/gcc/aarch64-linux-gnu/4.9/include/arm_neon.h
vmull_p64 (poly64_t a, poly64_t b)
vmull_high_p64 (poly64x2_t a, poly64x2_t b)
$

An Raspberry Pi 3 with ARMv8/Aarch32 and GCC 4.9.2 has it in arm_neon.h:

$ cat /usr/lib/gcc/arm-linux-gnueabihf/4.9.2/include/arm_neon.h | grep
-A 4 vreinterpretq_u64_p128
vreinterpretq_u64_p128 (poly128_t __a)
{
  return (uint64x2_t)__builtin_neon_vreinterpretv2diti
((__builtin_neon_ti) __a);
}

*****

Linaro machine:

$ gcc -v
Using built-in specs.
COLLECT_GCC=gcc
COLLECT_LTO_WRAPPER=/usr/lib/gcc/aarch64-linux-gnu/4.9/lto-wrapper
Target: aarch64-linux-gnu
Configured with: ../src/configure -v --with-pkgversion='Debian/Linaro 4.9.2-10'
--with-bugurl=file:///usr/share/doc/gcc-4.9/README.Bugs
--enable-languages=c,c++,java,go,d,fortran,objc,obj-c++ --prefix=/usr
--program-suffix=-4.9 --enable-shared --enable-linker-build-id
--libexecdir=/usr/lib --without-included-gettext --enable-threads=posix
--with-gxx-include-dir=/usr/include/c++/4.9 --libdir=/usr/lib --enable-nls
--with-sysroot=/ --enable-clocale=gnu --enable-libstdcxx-debug
--enable-libstdcxx-time=yes --enable-gnu-unique-object --disable-libsanitizer
--disable-libquadmath --enable-plugin --with-system-zlib
--disable-browser-plugin --enable-java-awt=gtk --enable-gtk-cairo
--with-java-home=/usr/lib/jvm/java-1.5.0-gcj-4.9-arm64/jre --enable-java-home
--with-jvm-root-dir=/usr/lib/jvm/java-1.5.0-gcj-4.9-arm64
--with-jvm-jar-dir=/usr/lib/jvm-exports/java-1.5.0-gcj-4.9-arm64
--with-arch-directory=arm64 --with-ecj-jar=/usr/share/java/eclipse-ecj.jar
--enable-multiarch --enable-checking=release --build=aarch64-linux-gnu
--host=aarch64-linux-gnu --target=aarch64-linux-gnu
Thread model: posix
gcc version 4.9.2 (Debian/Linaro 4.9.2-10)