Skip site navigation (1)Skip section navigation (2)
Date:      Sun, 18 Jun 2017 23:46:25 -0700
From:      Mark Millard <markmi@dsl-only.net>
To:        freebsd-arm <freebsd-arm@freebsd.org>, FreeBSD Toolchain <freebsd-toolchain@freebsd.org>
Subject:   arm64 on head -r320059 (e.g.) fails buildkernel with only kernel-toolchain first (not buildworld) [Bugzilla 220125]
Message-ID:  <9B6857F6-FD8E-43B7-B142-050E51EE68AB@dsl-only.net>

next in thread | raw e-mail | index | archive | help
This is a variant of the wording in bugzilla 220125:

Unless buildworld (not just kernel-toolchain) is used before
buildkernel the result for arm64 is:

--- 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
#include <stdint.h>
         ^~~~~~~~~~
--- all_subdir_armv8crypto ---
*** [armv8_crypto_wrap.o] Error code 1

Doing a kernel-toolchain build establishes:

# ls -dlT /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/include/*
drwxr-xr-x  2 root  wheel  2 Jun 18 22:14:57 2017
/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/include/arpa
drwxr-xr-x  2 root  wheel  2 Jun 18 22:14:59 2017
/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/include/gssapi
drwxr-xr-x  2 root  wheel  2 Jun 18 22:14:57 2017
/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/include/protocols
drwxr-xr-x  2 root  wheel  2 Jun 18 22:14:58 2017
/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/include/rpc
drwxr-xr-x  2 root  wheel  2 Jun 18 22:14:58 2017
/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/include/rpcsvc
drwxr-xr-x  2 root  wheel  2 Jun 18 22:14:59 2017
/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/include/xlocale

which excludes the following that a buildworld establishes
(shown from a different build):

# find /usr/obj/cortexA53_clang/ -name stdint.h -print | more
=
/usr/obj/cortexA53_clang/arm64.aarch64/usr/src/tmp/usr/include/sys/stdint.=
h
=
/usr/obj/cortexA53_clang/arm64.aarch64/usr/src/tmp/usr/include/c++/v1/stdi=
nt.h
=
/usr/obj/cortexA53_clang/arm64.aarch64/usr/src/tmp/usr/include/c++/v1/tr1/=
stdint.h
/usr/obj/cortexA53_clang/arm64.aarch64/usr/src/tmp/usr/include/stdint.h

One of:

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 )

at least if the kernel-toolchain then buildkernel
sequence is to be supported for arm64.


=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?9B6857F6-FD8E-43B7-B142-050E51EE68AB>