aarch64-arm64 fails to build kernel 12-current raspberry pi 3
Brian Scott
bscott at bunyatech.com.au
Wed Jul 11 12:10:36 UTC 2018
Same happened to me on 336007 last week. I put armv8crypto into
WITHOUT_MODULES in make.conf because I needed the build for other reasons.
I guess builds on other archs wouldn't be building armv8 stuff.
Brian
On 11/7/18 9:42 pm, tech-lists wrote:
> 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
>
>
More information about the freebsd-arm
mailing list