Date: Wed, 11 Jul 2018 22:10:25 +1000 From: Brian Scott <bscott@bunyatech.com.au> To: freebsd-arm@freebsd.org Subject: Re: aarch64-arm64 fails to build kernel 12-current raspberry pi 3 Message-ID: <65245a1f-1457-6c2e-699e-132af53adf0e@bunyatech.com.au> In-Reply-To: <a68f6312-c9a3-2e5e-2216-bfa3b1df9a70@zyxst.net> References: <a68f6312-c9a3-2e5e-2216-bfa3b1df9a70@zyxst.net>
next in thread | previous in thread | raw e-mail | index | archive | help
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@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 > >
Want to link to this message? Use this URL: <https://mail-archive.FreeBSD.org/cgi/mid.cgi?65245a1f-1457-6c2e-699e-132af53adf0e>