From owner-freebsd-arm@freebsd.org Fri Oct 20 05:32:20 2017 Return-Path: Delivered-To: freebsd-arm@mailman.ysv.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by mailman.ysv.freebsd.org (Postfix) with ESMTP id 64467E50429 for ; Fri, 20 Oct 2017 05:32:20 +0000 (UTC) (envelope-from markmi@dsl-only.net) Received: from asp.reflexion.net (outbound-mail-210-80.reflexion.net [208.70.210.80]) (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 191F76922A for ; Fri, 20 Oct 2017 05:32:19 +0000 (UTC) (envelope-from markmi@dsl-only.net) Received: (qmail 5398 invoked from network); 20 Oct 2017 05:32:12 -0000 Received: from unknown (HELO rtc-sm-01.app.dca.reflexion.local) (10.81.150.1) by 0 (rfx-qmail) with SMTP; 20 Oct 2017 05:32:12 -0000 Received: by rtc-sm-01.app.dca.reflexion.local (Reflexion email security v8.40.3) with SMTP; Fri, 20 Oct 2017 01:32:12 -0400 (EDT) Received: (qmail 31131 invoked from network); 20 Oct 2017 05:32:12 -0000 Received: from unknown (HELO iron2.pdx.net) (69.64.224.71) by 0 (rfx-qmail) with (AES256-SHA encrypted) SMTP; 20 Oct 2017 05:32:12 -0000 Received: from [192.168.1.25] (c-76-115-7-162.hsd1.or.comcast.net [76.115.7.162]) by iron2.pdx.net (Postfix) with ESMTPSA id B9794EC8166; Thu, 19 Oct 2017 22:32:11 -0700 (PDT) From: Mark Millard Content-Type: text/plain; charset=us-ascii Content-Transfer-Encoding: quoted-printable Mime-Version: 1.0 (Mac OS X Mail 10.3 \(3273\)) Subject: Re: Spot of bother compiling an ARMv8 kernel... Date: Thu, 19 Oct 2017 22:32:10 -0700 References: To: Jon Brawn , freebsd-arm , FreeBSD Toolchain In-Reply-To: Message-Id: <63A81F33-4DAF-45A3-A19A-F83FE63DB331@dsl-only.net> X-Mailer: Apple Mail (2.3273) X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.23 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 20 Oct 2017 05:32:20 -0000 On 2017-Oct-19, at 9:25 PM, Jon Brawn wrote: . . . > root@brax:/usr/src # make TARGET=3Darm64 TARGET_ARCH=3Daarch64 = KERNCONF=3DGENERIC-NODEBUG kernel >=20 > And off it went. >=20 > Then, alas, it stopped: >=20 > cc -target aarch64-unknown-freebsd12.0 --sysroot=3D/usr/obj/usr/src/tmp = -B/usr/obj/usr/src/tmp/usr/bin -c -O3 -pipe -fno-strict-aliasing -Werror = -D_KERNEL -DKLD_MODULE -DHAVE_KERNEL_OPTION_HEADERS -include = /usr/obj/usr/src/sys/GENERIC-NODEBUG/opt_global.h -I. -I/usr/src/sys = -fno-common -g -fPIC -I/usr/obj/usr/src/sys/GENERIC-NODEBUG -ffixed-x18 = -ffreestanding -fwrapv -fstack-protector -gdwarf-2 -Wall = -Wredundant-decls -Wnested-externs -Wstrict-prototypes = -Wmissing-prototypes -Wpointer-arith -Winline -Wcast-qual -Wundef = -Wno-pointer-sign -D__printf__=3D__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-error-address-of-packed-member -std=3Diso9899:1999 -Werror = -march=3Darmv8-a+crypto /usr/src/sys/crypto/armv8/armv8_crypto_wrap.c > In file included from = /usr/src/sys/crypto/armv8/armv8_crypto_wrap.c:46: > /usr/lib/clang/5.0.0/include/arm_neon.h:31:10: fatal error: 'stdint.h' = file not > found > #include > ^~~~~~~~~~ > 1 error generated. > *** Error code 1 . . . See also: bugzilla 220125 from back in 2017-Jun-19. Normally the kernel does not depend on stdint.h but for this arm NOEN code it does. make . . . buildworld buildkernel would work: the buildworld would put the stdint.h in a place where the buidlkernel would find it. Unfortunately, make . . . kernel-toolchain make . . . buildkernel would not put the stdint.h in a place that buildkernel would fine it --and, so, it would error out the same way. =3D=3D=3D Mark Millard markmi at dsl-only.net