From owner-freebsd-arm@freebsd.org Fri Oct 20 05:08:47 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 73B2EE4FE0A for ; Fri, 20 Oct 2017 05:08:47 +0000 (UTC) (envelope-from jon@brawn.org) Received: from ahs1.r4l.com (ahs1.r4l.com [198.27.81.125]) (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 487126816A for ; Fri, 20 Oct 2017 05:08:46 +0000 (UTC) (envelope-from jon@brawn.org) DKIM-Signature: v=1; a=rsa-sha256; q=dns/txt; c=relaxed/relaxed; d=brawn.org; s=default; h=To:Date:Message-Id:Subject:Mime-Version:Content-Type:From: Sender:Reply-To:Cc:Content-Transfer-Encoding:Content-ID:Content-Description: Resent-Date:Resent-From:Resent-Sender:Resent-To:Resent-Cc:Resent-Message-ID: In-Reply-To:References:List-Id:List-Help:List-Unsubscribe:List-Subscribe: List-Post:List-Owner:List-Archive; bh=LYB+eeW8XL/RF10EVwDO0fmGHZ+GNg1rHS9+gPcEMX8=; b=w7rXjGk2BMHS/sSB7puoIWa4N4 tZn7UA/Cv3TjK0BnJkNrx4PR3Nb4xwN8HCwxKAY6sng53PArNz7gFhdhV60jrBDe4+3NBgnvz9Ofx 8OBHm+krM/5w2/SYPXhaYrc6uZKNpsCOoprosHTbcKmgmQOyLyMiw4YyD1urMXwfQxU571XAMeAz+ I3UIAyVBG5QVG0emfjCOh9R7Udg+IQJhV3iW0hBagjoh4trKez55MryOCSxKVdhjrkzolnqhPaT4h d9wLEg5DnDCOLAMBA1CTzOb8kS3i523lMbfbXE/pu6JgyzUvly+7mRc+TqHL71a9XDiA/5BTWMZ0M 1zSvEP+g==; Received: from [136.62.171.86] (port=55980 helo=[192.168.1.159]) by ahs1.r4l.com with esmtpsa (TLSv1.2:ECDHE-RSA-AES256-GCM-SHA384:256) (Exim 4.89) (envelope-from ) id 1e5OsV-001roy-FW for freebsd-arm@freebsd.org; Fri, 20 Oct 2017 00:25:47 -0400 From: Jon Brawn Mime-Version: 1.0 (Mac OS X Mail 10.3 \(3273\)) Subject: Spot of bother compiling an ARMv8 kernel... Message-Id: Date: Thu, 19 Oct 2017 23:25:45 -0500 To: freebsd-arm@freebsd.org X-Mailer: Apple Mail (2.3273) X-AntiAbuse: This header was added to track abuse, please include it with any abuse report X-AntiAbuse: Primary Hostname - ahs1.r4l.com X-AntiAbuse: Original Domain - freebsd.org X-AntiAbuse: Originator/Caller UID/GID - [47 12] / [47 12] X-AntiAbuse: Sender Address Domain - brawn.org X-Get-Message-Sender-Via: ahs1.r4l.com: authenticated_id: jon@brawn.org X-Authenticated-Sender: ahs1.r4l.com: jon@brawn.org X-Source: X-Source-Args: X-Source-Dir: Content-Type: text/plain; charset=utf-8 Content-Transfer-Encoding: quoted-printable X-Content-Filtered-By: Mailman/MimeDel 2.1.23 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:08:47 -0000 Wotcha! I=E2=80=99ve got use of a SoftIron OverDrive 1000, and I thought it was = about time I updated it to a newer version of 12.0 CURRENT, so I = dutifully downloaded the mini memory stick image, installed all the = options that the installer offers, rebooted off of the hard drive, and = decided that the first thing that one has to do with a new system is = build a spangly new kernel. So: root@brax:/usr/src # make TARGET=3Darm64 TARGET_ARCH=3Daarch64 = KERNCONF=3DGENERIC-NODEBUG kernel And off it went. Then, alas, it stopped: 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 Stop. What is the freebsd-arm protocol for dealing with this kind of issue? Do = I file a bugzilla on it? Or just ask nicely on this list, and someone = will say, =E2=80=9CAh, yes, you need to install and everything = will be alright. Must remember to put that on my to-do list!=E2=80=9D? I = can work around it easily enough using =E2=80=9CThe Mark Of Brawn=E2=80=9D= (what others might call, less charitably, =E2=80=9Ca bodge=E2=80=9D). Jon.=