From owner-freebsd-toolchain@freebsd.org Wed Jun 21 06:33:42 2017 Return-Path: Delivered-To: freebsd-toolchain@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 8BBB0D87A73; Wed, 21 Jun 2017 06:33:42 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from tensor.andric.com (tensor.andric.com [IPv6:2001:470:7a58:1::1]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client CN "tensor.andric.com", Issuer "COMODO RSA Domain Validation Secure Server CA" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 4A46582315; Wed, 21 Jun 2017 06:33:42 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from [IPv6:2001:470:7a58::9566:2e4e:8fb0:5a26] (unknown [IPv6:2001:470:7a58:0:9566:2e4e:8fb0:5a26]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by tensor.andric.com (Postfix) with ESMTPSA id EDE581DF4D; Wed, 21 Jun 2017 08:33:39 +0200 (CEST) From: Dimitry Andric Message-Id: Content-Type: multipart/signed; boundary="Apple-Mail=_51A3155A-FCF3-4593-ABDA-71EC2D149934"; protocol="application/pgp-signature"; micalg=pgp-sha1 Mime-Version: 1.0 (Mac OS X Mail 10.3 \(3273\)) Subject: Re: arm64 on head -r320059 (e.g.) fails buildkernel with only kernel-toolchain first (not buildworld) [Bugzilla 220125] Date: Wed, 21 Jun 2017 08:33:36 +0200 In-Reply-To: Cc: freebsd-arm , FreeBSD Toolchain To: Ryan Stone References: <9B6857F6-FD8E-43B7-B142-050E51EE68AB@dsl-only.net> X-Mailer: Apple Mail (2.3273) X-BeenThere: freebsd-toolchain@freebsd.org X-Mailman-Version: 2.1.23 Precedence: list List-Id: Maintenance of FreeBSD's integrated toolchain List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 21 Jun 2017 06:33:42 -0000 --Apple-Mail=_51A3155A-FCF3-4593-ABDA-71EC2D149934 Content-Transfer-Encoding: 7bit Content-Type: text/plain; charset=us-ascii On 21 Jun 2017, at 02:15, Ryan Stone wrote: > > On Mon, Jun 19, 2017 at 2:57 AM, Dimitry Andric wrote: > >> Solution B is problematic because arm_neon.h uses stdint.h types >> extensively. >> > > If I manually modify the arm_neon.h file to instead say this, the problem > is avoided and the kernel builds: > > #ifdef _KERNEL > #include > #else > #include > #endif > > Do you think that the llvm devs would be willing to take a change to > NeonEmitter that does this on FreeBSD? > > This may not be a complete solution, though, as googling seems to indicate > that gcc also provides a arm_neon.h and it also #includes Indeed. It seems this header is not really designed to be included from kernel space. It is probably easiest to provide a kernel wrapper for stdint.h, maybe even just for arm. -Dimitry --Apple-Mail=_51A3155A-FCF3-4593-ABDA-71EC2D149934 Content-Transfer-Encoding: 7bit Content-Disposition: attachment; filename=signature.asc Content-Type: application/pgp-signature; name=signature.asc Content-Description: Message signed with OpenPGP -----BEGIN PGP SIGNATURE----- Version: GnuPG/MacGPG2 v2.0.30 iEYEARECAAYFAllKE0QACgkQsF6jCi4glqPmYwCgr4kvpP675xDZQosA5G3yBjth o3MAn0OIRqqxHMmorkvJxWo418O6avkm =/4Xt -----END PGP SIGNATURE----- --Apple-Mail=_51A3155A-FCF3-4593-ABDA-71EC2D149934--