Skip site navigation (1)Skip section navigation (2)
Date:      Thu, 19 Oct 2017 22:32:10 -0700
From:      Mark Millard <markmi@dsl-only.net>
To:        Jon Brawn <jon@brawn.org>, freebsd-arm <freebsd-arm@freebsd.org>, FreeBSD Toolchain <freebsd-toolchain@freebsd.org>
Subject:   Re: Spot of bother compiling an ARMv8 kernel...
Message-ID:  <63A81F33-4DAF-45A3-A19A-F83FE63DB331@dsl-only.net>
In-Reply-To: <EB2BA2D9-8242-44D2-9028-B054CB378922@brawn.org>
References:  <EB2BA2D9-8242-44D2-9028-B054CB378922@brawn.org>

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

On 2017-Oct-19, at 9:25 PM, Jon Brawn <jon@brawn.org> 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 <stdint.h>
>         ^~~~~~~~~~
> 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




Want to link to this message? Use this URL: <https://mail-archive.FreeBSD.org/cgi/mid.cgi?63A81F33-4DAF-45A3-A19A-F83FE63DB331>