From owner-freebsd-arm@freebsd.org Wed Jul 11 12:10:36 2018 Return-Path: Delivered-To: freebsd-arm@mailman.ysv.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.ysv.freebsd.org (Postfix) with ESMTP id 88ACE103496F for ; Wed, 11 Jul 2018 12:10:36 +0000 (UTC) (envelope-from bscott@bunyatech.com.au) Received: from ppp150-101-221-139.static.internode.on.net (2001-44b8-4170-0a00-0000-0000-0000-0002.static.ipv6.internode.on.net [IPv6:2001:44b8:4170:a00::2]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client CN "150.101.221.139", Issuer "Bunya Technology Certification Authority" (not verified)) by mx1.freebsd.org (Postfix) with ESMTPS id A85A58E589 for ; Wed, 11 Jul 2018 12:10:34 +0000 (UTC) (envelope-from bscott@bunyatech.com.au) X-Clacks-Overhead: GNU Terry Pratchett Received: from DHCP.tawonga.bunyatech.com.au (DHCP.tawonga.bunyatech.com.au [10.0.1.78] (may be forged)) (authenticated bits=0) by cope.tawonga.bunyatech.com.au (8.15.2/8.15.2/MSA) with ESMTPSA id w6BCAPF6018215 (version=TLSv1.2 cipher=ECDHE-RSA-AES128-GCM-SHA256 bits=128 verify=OK) for ; Wed, 11 Jul 2018 22:10:27 +1000 (AEST) (envelope-from bscott@bunyatech.com.au) Subject: Re: aarch64-arm64 fails to build kernel 12-current raspberry pi 3 To: freebsd-arm@freebsd.org References: From: Brian Scott Message-ID: <65245a1f-1457-6c2e-699e-132af53adf0e@bunyatech.com.au> Date: Wed, 11 Jul 2018 22:10:25 +1000 User-Agent: Mozilla/5.0 (Macintosh; Intel Mac OS X 10.13; rv:52.0) Gecko/20100101 Thunderbird/52.9.1 MIME-Version: 1.0 In-Reply-To: Content-Type: text/plain; charset=utf-8 Content-Transfer-Encoding: 8bit Content-Language: en-US X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.27 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 11 Jul 2018 12:10:36 -0000 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 >          ^~~~~~~~~~ > 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 > >