Skip site navigation (1)Skip section navigation (2)
Date:      Mon, 19 Jun 2017 08:57:57 +0200
From:      Dimitry Andric <dim@FreeBSD.org>
To:        Mark Millard <markmi@dsl-only.net>
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:  <CB7359D7-4BFE-45A8-838A-AA69B9450398@FreeBSD.org>
In-Reply-To: <9B6857F6-FD8E-43B7-B142-050E51EE68AB@dsl-only.net>
References:  <9B6857F6-FD8E-43B7-B142-050E51EE68AB@dsl-only.net>

next in thread | previous in thread | raw e-mail | index | archive | help

--Apple-Mail=_8BCD7550-BEF8-4E57-9A25-5FBD27DC51AB
Content-Transfer-Encoding: quoted-printable
Content-Type: text/plain;
	charset=us-ascii

On 19 Jun 2017, at 08:46, Mark Millard <markmi@dsl-only.net> wrote:
>=20
> This is a variant of the wording in bugzilla 220125:
>=20
> Unless buildworld (not just kernel-toolchain) is used before
> buildkernel the result for arm64 is:
>=20
> --- armv8_crypto_wrap.o ---
> In file included from =
/usr/src/sys/crypto/armv8/armv8_crypto_wrap.c:46:
> =
/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/usr/bin/../lib/clang=
/4.0.0/include/arm_neon.h:31:10:
> fatal error: 'stdint.h' file not found
...
> A) kernel-toolchain needs to establish a stdint.h
>   that would be found
> vs.
> B) arm_neon.h needs to avoid needing stdint.h
>   (presumes armv8_crypto_wrap.c is correct to
>    include arm_neon.h )
>=20
> at least if the kernel-toolchain then buildkernel
> sequence is to be supported for arm64.

Solution A is problematic because it then would require to install
headers into ${WORLDTMP}.  This is what buildworld does.

Solution B is problematic because arm_neon.h uses stdint.h types
extensively.

Maybe the solution with the least amount of work is to provide a
kernel-specific wrapper header with the stdint.h types.

Otherwise, just use buildworld before buildkernel.

-Dimitry


--Apple-Mail=_8BCD7550-BEF8-4E57-9A25-5FBD27DC51AB
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

iEYEARECAAYFAllHdgEACgkQsF6jCi4glqNR/gCZAXSo9eVtCuqjIVeKgs/XMEtg
7u4AoIwiE22tjwL/5g06Txfrqv2mtf0y
=Qfey
-----END PGP SIGNATURE-----

--Apple-Mail=_8BCD7550-BEF8-4E57-9A25-5FBD27DC51AB--



Want to link to this message? Use this URL: <https://mail-archive.FreeBSD.org/cgi/mid.cgi?CB7359D7-4BFE-45A8-838A-AA69B9450398>