kernel build fails on arm64

[Thadeu Lima de Souza Cascardo]

After upgrading gcc-7-aarch64-linux-gnu from (7.3.0-12ubuntu1cross1) to (7.3.0-11ubuntu1cross1), we get:

In file included from lib/raid6/recov_neon_inner.c:11:0:
/usr/lib/gcc-cross/aarch64-linux-gnu/7/include/arm_neon.h: In function ‘vdot_lane_u32’:
/usr/lib/gcc-cross/aarch64-linux-gnu/7/include/arm_neon.h:31581:10: error: incompatible types when returning type ‘int’ but ‘uint32x2_t’ was expected
   return __builtin_aarch64_udot_lanev8qi_uuuus (__r, __a, __b, __index);
          ^
/usr/lib/gcc-cross/aarch64-linux-gnu/7/include/arm_neon.h: In function ‘vdot_laneq_u32’:
/usr/lib/gcc-cross/aarch64-linux-gnu/7/include/arm_neon.h:31589:10: error: incompatible types when returning type ‘int’ but ‘uint32x2_t’ was expected
   return __builtin_aarch64_udot_laneqv8qi_uuuus (__r, __a, __b, __index);
          ^
/usr/lib/gcc-cross/aarch64-linux-gnu/7/include/arm_neon.h: In function ‘vdotq_lane_u32’:
/usr/lib/gcc-cross/aarch64-linux-gnu/7/include/arm_neon.h:31597:10: error: incompatible types when returning type ‘int’ but ‘uint32x4_t’ was expected
   return __builtin_aarch64_udot_lanev16qi_uuuus (__r, __a, __b, __index);
          ^
/usr/lib/gcc-cross/aarch64-linux-gnu/7/include/arm_neon.h: In function ‘vdotq_laneq_u32’:
/usr/lib/gcc-cross/aarch64-linux-gnu/7/include/arm_neon.h:31605:10: error: incompatible types when returning type ‘int’ but ‘uint32x4_t’ was expected
   return __builtin_aarch64_udot_laneqv16qi_uuuus (__r, __a, __b, __index);
          ^
scripts/Makefile.build:324: recipe for target 'lib/raid6/recov_neon_inner.o' failed
make[2]: *** [lib/raid6/recov_neon_inner.o] Error 1

Cascardo.

[Matthias Klose (doko)]

please recheck with the current native gcc-7 in -proposed

[Matthias Klose (doko)]

and more:

 - what was the last version not having this issue?
 - please provide the preprocessed source and the command line
   options to reproduce the issue.

[Thadeu Lima de Souza Cascardo (cascardo)]

I am not sure if there was something after 7.3.0-11ubuntu1cross1, but it worked for me.

I just ran the command below and reproduced the bug. I will attach the code.

aarch64-linux-gnu-gcc -c recov_neon_inner.c

[Thadeu Lima de Souza Cascardo (cascardo)]

By the way, native building works fine.

[Seth Forshee (sforshee)]

I tested a cross build with gcc-7-cross 18ubuntu2, still fails in the same way.

[Thadeu Lima de Souza Cascardo (cascardo)]

7.3.0-13ubuntu1cross1 still fails.

[Maxim Kuvyrkov (maxim-kuvyrkov)]

Tentative fix applied, see bugs.linaro.org #3718 .

[Thadeu Lima de Souza Cascardo (cascardo)]

7.3.0-15ubuntu1cross1 was working, but 7.3.0-15ubuntu2cross1 regressed, and it still fails.

Cascardo.

[Launchpad Janitor (janitor)]

This bug was fixed in the package gcc-7 - 7.3.0-16ubuntu2

---------------
gcc-7 (7.3.0-16ubuntu2) bionic; urgency=medium

  * Merge with Debian; remaining changes:
    - Build from upstream sources.
  * Update the gcc-foffload-default patch. LP: #1721355.

gcc-7 (7.3.0-16) unstable; urgency=medium

  * Update to SVN 20180411 (r259316) from the gcc-7-branch.
    - Fix PR target/85203 (ARM), PR target/84748 (AArch64), PR c++/85279,
      PR target/85196 (SPARC).
  * Use triplet-prefixed as and ld (Helmut Grohne). Addresses: #895251.
  * Link libasan, liblsan, libubsan always with --no-as-needed. LP: #1762683.
  * Backport r251558 from the trunk, addresses Linaro #3718. LP: #1759369.
  * Fix PR libstdc++/85222, taken from the trunk.
  * Use --push-state --as-needed and --pop-state instead of --as-needed and
    --no-as-needed for linking libgcc.

 -- Matthias Klose <email address hidden> Thu, 12 Apr 2018 00:45:22 +0200

[Launchpad Janitor (janitor)]

This bug was fixed in the package gcc-7-cross - 20ubuntu3

---------------
gcc-7-cross (20ubuntu3) bionic; urgency=medium

  * Build using 7.3.0-16ubuntu1.
  * Backport r251558 from the trunk, addresses Linaro #3718. LP: #1759369.

 -- Matthias Klose <email address hidden> Wed, 11 Apr 2018 22:29:32 +0200