From owner-freebsd-current@freebsd.org Wed Jul 11 11:42:58 2018 Return-Path: Delivered-To: freebsd-current@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 021E81030D45; Wed, 11 Jul 2018 11:42:58 +0000 (UTC) (envelope-from tech-lists@zyxst.net) Received: from out1-smtp.messagingengine.com (out1-smtp.messagingengine.com [66.111.4.25]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id 9C26E8CC47; Wed, 11 Jul 2018 11:42:57 +0000 (UTC) (envelope-from tech-lists@zyxst.net) Received: from compute4.internal (compute4.nyi.internal [10.202.2.44]) by mailout.nyi.internal (Postfix) with ESMTP id 00E9E20FAD; Wed, 11 Jul 2018 07:42:57 -0400 (EDT) Received: from mailfrontend1 ([10.202.2.162]) by compute4.internal (MEProxy); Wed, 11 Jul 2018 07:42:57 -0400 DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=zyxst.net; h=cc :content-transfer-encoding:content-type:date:from:message-id :mime-version:subject:to:x-me-sender:x-me-sender:x-sasl-enc; s= fm3; bh=grd00StZFjYRV2JhI8bO4K6Ux271Wjh3unsDzk81i+E=; b=qWhnS58z i53wLYdRBwmbi9cG8SUfi36lfQCoFdA2RVyz4kHlhRQFyaPUpdKp+XzaT5+XiYw4 mmdc0v2X3zDgWBcknuVFjtuWjUVmRpEuWhx8HZ34UQgyjBNwzxKb57QD7D176sc+ AP77GH8OgNPE8xww0dbYYKelqmG7jmsu62k/s3hy1PP5/PkfCPIjSDk/5ddEoQD1 wGNiMRLFru3HFXchTWIbh4a+QK63qUkswSGOXxlBVf5zX1GS9+b90Ml5/rbyEQVy 4tzWjiqsVsY6LzMPc+wmU98HjvB49IgUJp95upfFDOezKv8CtuwKfBEQtNt457h/ N0Qhy+SiiJ3Y0g== DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d= messagingengine.com; h=cc:content-transfer-encoding:content-type :date:from:message-id:mime-version:subject:to:x-me-sender :x-me-sender:x-sasl-enc; s=fm3; bh=grd00StZFjYRV2JhI8bO4K6Ux271W jh3unsDzk81i+E=; b=idEsUhA+3FsOWzwGLDjXhRUuEPW47Djsr7Xyjnl/Bmr0C TEhTox/TK/rtw546eJ0es8WIcpruE/PHWBTvDGIvMpwlf/gL1SROmDMq5HG2hgID zTF+IY7E/YuNsWZ9IttZKCYMeVyRA0rbngdIRQlUyMhSUw3xV365ejW05RQECnPw 4C+guYDHYe5/zbmMlzxdtxhSP2GJH05rxA4sU9AId+FlqEmaAdUb+ISQCXiafnKD NapR6fggUPvV11tBbO8VsPCoMNHda2pa4lo318SEggXe07htmKcug60mkQAm0pKa t52UI1B6czk3A4uNQD4yPLENGCYmgX2ynuA+JcyCw== X-ME-Proxy: X-ME-Sender: Received: from desktop.local (parsley.growveg.org [82.70.91.97]) by mail.messagingengine.com (Postfix) with ESMTPA id 3D574E4072; Wed, 11 Jul 2018 07:42:56 -0400 (EDT) To: freebsd-arm@freebsd.org Cc: FreeBSD Current From: tech-lists Subject: aarch64-arm64 fails to build kernel 12-current raspberry pi 3 Organization: none Message-ID: Date: Wed, 11 Jul 2018 12:42:54 +0100 User-Agent: Mozilla/5.0 (X11; FreeBSD amd64; rv:52.0) Gecko/20100101 Thunderbird/52.9.0 MIME-Version: 1.0 Content-Type: text/plain; charset=utf-8; format=flowed Content-Language: en-US Content-Transfer-Encoding: 7bit X-BeenThere: freebsd-current@freebsd.org X-Mailman-Version: 2.1.27 Precedence: list List-Id: Discussions about the use of FreeBSD-current List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 11 Jul 2018 11:42:58 -0000 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 -- J.