Linaro GCC

kernel build fails on arm64

Bug #1759369 reported by Thadeu Lima de Souza Cascardo on 2018-03-27

This bug affects 4 people

	Status	Importance	Assigned to
Linaro GCC	Fix Released	High	bugs.linaro.org #3718
gcc-7 (Ubuntu)	Fix Released	Undecided	Unassigned
Bionic	Fix Released	Undecided	Unassigned
gcc-7-cross (Ubuntu)	Fix Released	High	Unassigned
Bionic	Fix Released	High	Unassigned

Bug Description

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.

Thadeu Lima de Souza Cascardo (cascardo) on 2018-03-27

Changed in gcc-7-cross (Ubuntu):
importance:	Undecided → High

Revision history for this message

Matthias Klose (doko) wrote on 2018-03-28:

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

Changed in gcc-7-cross (Ubuntu):
status:	New → Incomplete

Revision history for this message

Matthias Klose (doko) wrote on 2018-03-28:

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.

Revision history for this message

Thadeu Lima de Souza Cascardo (cascardo) wrote on 2018-03-28:

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

Revision history for this message

Thadeu Lima de Souza Cascardo (cascardo) wrote on 2018-03-28:

code that breaks Edit (2.6 KiB, text/x-csrc)

Revision history for this message

Thadeu Lima de Souza Cascardo (cascardo) wrote on 2018-03-28:

By the way, native building works fine.

Revision history for this message

Seth Forshee (sforshee) wrote on 2018-03-29:

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

Matthias Klose (doko) on 2018-04-03

Changed in gcc-7-cross (Ubuntu):
status:	Incomplete → Confirmed

Bug Watch Updater (bug-watch-updater) on 2018-04-03

Changed in gcc-linaro:
importance:	Unknown → High
status:	Unknown → New

Revision history for this message

Thadeu Lima de Souza Cascardo (cascardo) wrote on 2018-04-03:

7.3.0-13ubuntu1cross1 still fails.

Revision history for this message

Maxim Kuvyrkov (maxim-kuvyrkov) wrote on 2018-04-11:

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

Revision history for this message

Thadeu Lima de Souza Cascardo (cascardo) wrote on 2018-04-11:

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

Cascardo.

Revision history for this message

Launchpad Janitor (janitor) wrote on 2018-04-13:

#10

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