aarch64-arm64 fails to build kernel 12-current raspberry pi 3

From: tech-lists <tech-lists_at_zyxst.net>
Date: Wed, 11 Jul 2018 12:42:54 +0100
Hello lists [x-posted to -current where it's also relevant]

12-current-arm64 fails to build generic-nodebug kernel

context:
12.0-CURRENT #0 r336134: Mon Jul  9 GENERIC arm64 (this is the older rpi3B+)

root_at_rpi3:/usr/src# svnlite info
Path: .
Working Copy Root Path: /ext/src
URL: https://svn.freebsd.org/base/head
Relative URL: ^/head
Repository Root: https://svn.freebsd.org/base
Repository UUID: ccf9f872-aa2e-dd11-9fc8-001c23d0bc1f
Revision: 336195
Node Kind: directory
Schedule: normal
Last Changed Author: eugen
Last Changed Rev: 336195
Last Changed Date: 2018-07-11 10:41:50 +0100 (Wed, 11 Jul 2018)

Some dirs on /usr are symlinked to a 1TB external disk. Swap is on the 
external disk. Made sure there was no src.conf or make.conf present:

root_at_rpi3:/root# cd /etc
root_at_rpi3:/etc# mv src.conf old.src.conf
root_at_rpi3:/etc# mv make.conf old.make.conf
root_at_rpi3:/etc# cd /usr/src

root_at_rpi3:/usr/src# rm -rf /ext/obj
root_at_rpi3:/usr/src# mkdir /ext/obj
root_at_rpi3:/usr/src# ls -lah /usr
total 72
drwxr-xr-x  12 root  wheel   512B Jul 10 11:15 .
drwxr-xr-x  20 root  wheel   512B Jul 10 18:45 ..
drwxr-xr-x   2 root  wheel   7.5K Jul  9 20:45 bin
drwxr-xr-x   2 root  wheel   512B Jul 10 11:15 home
drwxr-xr-x  56 root  wheel   6.5K Jul  9 20:44 include
drwxr-xr-x  10 root  wheel    16K Jul  9 20:45 lib
drwxr-xr-x   5 root  wheel   512B Jul  9 20:28 lib32
drwxr-xr-x   5 root  wheel   512B Jul  9 20:28 libdata
drwxr-xr-x   9 root  wheel   1.5K Jul  9 20:45 libexec
lrwxr-xr-x   1 root  wheel    10B Jul 10 11:43 local -> /ext/local
lrwxr-xr-x   1 root  wheel     8B Jul 10 11:41 obj -> /ext/obj
lrwxr-xr-x   1 root  wheel    10B Jul 10 11:41 ports -> /ext/ports
drwxr-xr-x   2 root  wheel   5.0K Jul  9 20:45 sbin
drwxr-xr-x  29 root  wheel   512B Jul  9 20:28 share
lrwxr-xr-x   1 root  wheel     8B Jul 10 11:41 src -> /ext/src
drwxr-xr-x  15 root  wheel   512B Jul  9 20:46 tests

root_at_rpi3:/usr/src# make -j10 cleanworld && make -j10 cleandir && make 
-j10 clean <--- just to make absolutely sure

[...]

RPI3 is just a copy of GENERIC-NODEBUG. it looks like this:

include GENERIC

ident   RPI3

nooptions       INVARIANTS
nooptions       INVARIANT_SUPPORT
nooptions       WITNESS
nooptions       WITNESS_SKIPSPIN
nooptions       DEADLKRES
nooptions       USB_DEBUG

root_at_rpi3:/usr/src# make -j1 buildkernel KERNCONF=RPI3

[...]

===> armv8crypto (all)
[Creating objdir 
/ext/obj/ext/src/arm64.aarch64/sys/RPI3/modules/ext/src/sys/modules/armv8crypto...]
machine -> /ext/src/sys/arm64/include
ln -sf /ext/obj/ext/src/arm64.aarch64/sys/RPI3/opt_bus.h opt_bus.h
awk -f /ext/src/sys/tools/makeobjops.awk /ext/src/sys/kern/device_if.m -h
awk -f /ext/src/sys/tools/makeobjops.awk /ext/src/sys/kern/bus_if.m -h
awk -f /ext/src/sys/tools/makeobjops.awk 
/ext/src/sys/opencrypto/cryptodev_if.m -h
cc -target aarch64-unknown-freebsd12.0 
--sysroot=/ext/obj/ext/src/arm64.aarch64/tmp 
-B/ext/obj/ext/src/arm64.aarch64/tmp/usr/bin -c -O2 -pipe 
-fno-strict-aliasing -Werror -D_KERNEL -DKLD_MODULE -DKLD_TIED -nostdinc 
-DHAVE_KERNEL_OPTION_HEADERS -include 
/ext/obj/ext/src/arm64.aarch64/sys/RPI3/opt_global.h -I. -I/ext/src/sys 
-I/ext/src/sys/contrib/ck/include -g -fPIC 
-I/ext/obj/ext/src/arm64.aarch64/sys/RPI3 -MD -MF.depend.genoffset.o 
-MTgenoffset.o -mgeneral-regs-only -ffixed-x18 -ffreestanding -fwrapv 
-fstack-protector -gdwarf-2 -Wall -Wredundant-decls -Wnested-externs 
-Wstrict-prototypes -Wmissing-prototypes -Wpointer-arith -Wcast-qual 
-Wundef -Wno-pointer-sign -D__printf__=__freebsd_kprintf__ 
-Wmissing-include-dirs -fdiagnostics-show-option -Wno-unknown-pragmas 
-Wno-error-tautological-compare -Wno-error-empty-body 
-Wno-error-parentheses-equality -Wno-error-unused-function 
-Wno-error-pointer-sign -Wno-error-shift-negative-value 
-Wno-address-of-packed-member -std=iso9899:1999 
/ext/src/sys/kern/genoffset.c
sh /ext/src/sys/kern/genoffset.sh genoffset.o > offset.inc
cc -target aarch64-unknown-freebsd12.0 
--sysroot=/ext/obj/ext/src/arm64.aarch64/tmp 
-B/ext/obj/ext/src/arm64.aarch64/tmp/usr/bin  -O2 -pipe 
-fno-strict-aliasing -Werror -D_KERNEL -DKLD_MODULE -DKLD_TIED -nostdinc 
   -DHAVE_KERNEL_OPTION_HEADERS -include 
/ext/obj/ext/src/arm64.aarch64/sys/RPI3/opt_global.h -I. -I/ext/src/sys 
-I/ext/src/sys/contrib/ck/include -fno-common -g -fPIC 
-I/ext/obj/ext/src/arm64.aarch64/sys/RPI3   -MD 
-MF.depend.armv8_crypto.o -MTarmv8_crypto.o -mgeneral-regs-only 
-ffixed-x18 -ffreestanding -fwrapv -fstack-protector -gdwarf-2 -Wall 
-Wredundant-decls -Wnested-externs -Wstrict-prototypes 
-Wmissing-prototypes -Wpointer-arith -Wcast-qual -Wundef 
-Wno-pointer-sign -D__printf__=__freebsd_kprintf__ 
-Wmissing-include-dirs -fdiagnostics-show-option -Wno-unknown-pragmas 
-Wno-error-tautological-compare -Wno-error-empty-body 
-Wno-error-parentheses-equality -Wno-error-unused-function 
-Wno-error-pointer-sign -Wno-error-shift-negative-value 
-Wno-address-of-packed-member    -std=iso9899:1999 -c 
/ext/src/sys/crypto/armv8/armv8_crypto.c -o armv8_crypto.o
ctfconvert -L VERSION -g armv8_crypto.o
cc -target aarch64-unknown-freebsd12.0 
--sysroot=/ext/obj/ext/src/arm64.aarch64/tmp 
-B/ext/obj/ext/src/arm64.aarch64/tmp/usr/bin -c -O3 -pipe 
-fno-strict-aliasing -Werror -D_KERNEL -DKLD_MODULE -DKLD_TIED 
-DHAVE_KERNEL_OPTION_HEADERS -include 
/ext/obj/ext/src/arm64.aarch64/sys/RPI3/opt_global.h -I. -I/ext/src/sys 
-I/ext/src/sys/contrib/ck/include -fno-common -g -fPIC 
-I/ext/obj/ext/src/arm64.aarch64/sys/RPI3 -ffixed-x18 -ffreestanding 
-fwrapv -fstack-protector -gdwarf-2 -Wall -Wredundant-decls 
-Wnested-externs -Wstrict-prototypes -Wmissing-prototypes 
-Wpointer-arith -Wcast-qual -Wundef -Wno-pointer-sign 
-D__printf__=__freebsd_kprintf__ -Wmissing-include-dirs 
-fdiagnostics-show-option -Wno-unknown-pragmas 
-Wno-error-tautological-compare -Wno-error-empty-body 
-Wno-error-parentheses-equality -Wno-error-unused-function 
-Wno-error-pointer-sign -Wno-error-shift-negative-value 
-Wno-address-of-packed-member -std=iso9899:1999  -Werror 
-march=armv8-a+crypto /ext/src/sys/crypto/armv8/armv8_crypto_wrap.c
In file included from /ext/src/sys/crypto/armv8/armv8_crypto_wrap.c:46:
/usr/lib/clang/6.0.1/include/arm_neon.h:31:10: fatal error: 'stdint.h' 
file not found
#include <stdint.h>
          ^~~~~~~~~~
1 error generated.
*** [armv8_crypto_wrap.o] Error code 1

make[4]: stopped in /ext/src/sys/modules/armv8crypto
1 error

make[4]: stopped in /ext/src/sys/modules/armv8crypto
*** [all_subdir_armv8crypto] Error code 2

make[3]: stopped in /ext/src/sys/modules
1 error

make[3]: stopped in /ext/src/sys/modules
*** [modules-all] Error code 2

make[2]: stopped in /ext/obj/ext/src/arm64.aarch64/sys/RPI3
1 error

make[2]: stopped in /ext/obj/ext/src/arm64.aarch64/sys/RPI3
*** [buildkernel] Error code 2

make[1]: stopped in /ext/src
1 error

make[1]: stopped in /ext/src
*** [buildkernel] Error code 2

make: stopped in /ext/src
1 error

make: stopped in /ext/src


-- 
J.
Received on Wed Jul 11 2018 - 09:42:58 UTC

This archive was generated by hypermail 2.4.0 : Wed May 19 2021 - 11:41:17 UTC