Date: Wed, 21 Jun 2017 08:33:36 +0200 From: Dimitry Andric <dim@FreeBSD.org> To: Ryan Stone <rysto32@gmail.com> Cc: freebsd-arm <freebsd-arm@freebsd.org>, FreeBSD Toolchain <freebsd-toolchain@freebsd.org> Subject: Re: arm64 on head -r320059 (e.g.) fails buildkernel with only kernel-toolchain first (not buildworld) [Bugzilla 220125] Message-ID: <E1D1A6E9-201F-432E-86B0-8775783327B5@FreeBSD.org> In-Reply-To: <CAFMmRNwioFT%2BLk=WBvUbL4T3O6f1n_98iz7UhPvqWUdnTKCqPA@mail.gmail.com> References: <9B6857F6-FD8E-43B7-B142-050E51EE68AB@dsl-only.net> <CB7359D7-4BFE-45A8-838A-AA69B9450398@FreeBSD.org> <CAFMmRNwioFT%2BLk=WBvUbL4T3O6f1n_98iz7UhPvqWUdnTKCqPA@mail.gmail.com>
next in thread | previous in thread | raw e-mail | index | archive | help
--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 <rysto32@gmail.com> wrote: > > On Mon, Jun 19, 2017 at 2:57 AM, Dimitry Andric <dim@freebsd.org> 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 <sys/types.h> > #else > #include <stdint.h> > #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 <stdint.h> 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--
Want to link to this message? Use this URL: <https://mail-archive.FreeBSD.org/cgi/mid.cgi?E1D1A6E9-201F-432E-86B0-8775783327B5>