Date: Wed, 11 Jul 2018 12:42:54 +0100 From: tech-lists <tech-lists@zyxst.net> To: freebsd-arm@freebsd.org Cc: FreeBSD Current <freebsd-current@freebsd.org> Subject: aarch64-arm64 fails to build kernel 12-current raspberry pi 3 Message-ID: <a68f6312-c9a3-2e5e-2216-bfa3b1df9a70@zyxst.net>
next in thread | raw e-mail | index | archive | help
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@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@rpi3:/root# cd /etc root@rpi3:/etc# mv src.conf old.src.conf root@rpi3:/etc# mv make.conf old.make.conf root@rpi3:/etc# cd /usr/src root@rpi3:/usr/src# rm -rf /ext/obj root@rpi3:/usr/src# mkdir /ext/obj root@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@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@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.
Want to link to this message? Use this URL: <https://mail-archive.FreeBSD.org/cgi/mid.cgi?a68f6312-c9a3-2e5e-2216-bfa3b1df9a70>