declare -x ABI="amd64" declare -x ABI_MIPS="" declare -x ABI_S390="" declare -x ABI_X86="64" declare -x ADAFLAGS="" declare -x ADA_TARGET="" declare -x ALLOW_TEST="network" declare -x ALSA_CARDS="" declare -x AMDGPU_TARGETS="" declare -x ANT_HOME="/usr/share/ant" declare -x APACHE2_MODULES="" declare -x APACHE2_MPMS="" declare -x ARCH="amd64" declare BDEPEND=$'\n\tsys-apps/kmod[tools]\n\tmodules-sign? (\n\t\tdev-libs/openssl\n\t\tvirtual/pkgconfig\n\t)\n' declare -x BINPKG_FORMAT="xpak" declare -x BINPKG_GPG_SIGNING_BASE_COMMAND="/usr/bin/flock /run/lock/portage-binpkg-gpg.lock /usr/bin/gpg --sign --armor [PORTAGE_CONFIG]" declare -x BINPKG_GPG_SIGNING_DIGEST="SHA512" declare -x BINPKG_GPG_VERIFY_BASE_COMMAND="/usr/bin/gpg --verify --batch --no-tty --no-auto-check-trustdb --status-fd 2 [PORTAGE_CONFIG] [SIGNATURE]" declare -x BINPKG_GPG_VERIFY_GPG_HOME="/etc/portage/gnupg" declare -x BOOTSTRAP_USE="unicode internal-glib pkg-config split-usr xml python_targets_python3_11 python_single_target_python3_11 multilib" declare -x CALLIGRA_FEATURES="" declare -x CAMERAS="" declare -x CARGO_TERM_COLOR="never" declare -x CBUILD="x86_64-pc-linux-gnu" declare -x CCASFLAGS="" declare -x CFLAGS="-O2 -pipe -march=native -fno-diagnostics-color" declare -x CFLAGS_amd64="-m64" declare -x CFLAGS_default declare -x CFLAGS_x32="-mx32" declare -x CFLAGS_x86="-m32 -mfpmath=sse" declare -- CHECKCONFIG_DONOTHING="" declare -x CHOST="x86_64-pc-linux-gnu" declare -x CHOST_amd64="x86_64-pc-linux-gnu" declare -x CHOST_default="x86_64-pc-linux-gnu" declare -x CHOST_x32="x86_64-pc-linux-gnux32" declare -x CHOST_x86="i686-pc-linux-gnu" declare -x CMAKE_COLOR_DIAGNOSTICS="OFF" declare -x CMAKE_COLOR_MAKEFILE="OFF" declare -x COLLECTD_PLUGINS="" declare -- CONFIG_CHECK=$'\n\t\tINET\n\t\tNET\n\t\tNET_UDP_TUNNEL\n\t\tDST_CACHE\n\t\tCRYPTO\n\t\tCRYPTO_AES\n\t\tCRYPTO_GCM\n\t\tCRYPTO_CHACHA20POLY1305' declare -x CPPFLAGS="" declare -x CPU_FLAGS_ARM="" declare -x CPU_FLAGS_PPC="" declare -x CPU_FLAGS_X86="" declare -x CTARGET_default="x86_64-pc-linux-gnu" declare -x CURL_SSL="" declare -x CXXFLAGS="-O2 -pipe -march=native -fno-diagnostics-color" declare -x DEFAULT_ABI="amd64" declare -x DEFINED_PHASES=" compile configure install postinst setup" declare DEPEND=$'\n\tvirtual/linux-sources\n' declare DESCRIPTION="OpenVPN Data Channel Offload in the linux kernel" declare -x DIROPTIONS="-m0755" declare -x EAPI="8" declare -x EGO_BUILD_FLAGS="-p 5" declare -x ELIBC="glibc" declare -x ENV_UNSET="CARGO_HOME DBUS_SESSION_BUS_ADDRESS DISPLAY GDK_PIXBUF_MODULE_FILE GOBIN GOPATH PERL5LIB PERL5OPT PERLPREFIX PERL_CORE PERL_MB_OPT PERL_MM_OPT XAUTHORITY XDG_CACHE_HOME XDG_CONFIG_HOME XDG_DATA_HOME XDG_RUNTIME_DIR XDG_STATE_HOME" declare -- EPOCHREALTIME="1692244848.154886" declare -- EPOCHSECONDS="1692244848" declare -x EXEOPTIONS="-m0755" declare -- E_IDEPEND=$'\n\tsys-apps/kmod[tools]\n' declare -x FCFLAGS="-O2 -pipe -march=native -fno-diagnostics-color" declare -x FETCHCOMMAND_SSH="bash -c \"x=\\\${2#ssh://} ; host=\\\${x%%/*} ; port=\\\${host##*:} ; host=\\\${host%:*} ; [[ \\\${host} = \\\${port} ]] && port= ; exec rsync --rsh=\\\"ssh \\\${port:+-p\\\${port}} \\\${3}\\\" -avP \\\"\\\${host}:/\\\${x#*/}\\\" \\\"\\\$1\\\"\" rsync \"\${DISTDIR}/\${FILE}\" \"\${URI}\" \"\${PORTAGE_SSH_OPTS}\"" declare -x FFLAGS="-O2 -pipe -march=native -fno-diagnostics-color" declare -x FFTOOLS="" declare -x GCC_COLORS="" declare -x GCC_SPECS="" declare -x GIT_PAGER="cat" declare -x GO19CONCURRENTCOMPILATION="0" declare -x GOMAXPROCS="5" declare -x GPG_VERIFY_GROUP_DROP="nogroup" declare -x GPG_VERIFY_USER_DROP="nobody" declare -x GPSD_PROTOCOLS="" declare -x GRUB_PLATFORMS="" declare -x GSETTINGS_BACKEND="dconf" declare HOMEPAGE="https://github.com/OpenVPN/ovpn-dco" declare IDEPEND=$'\n\tsys-apps/kmod[tools]\n' declare -x INHERITED=" toolchain-funcs multilib flag-o-matic edo linux-info multiprocessing linux-mod-r1" declare -x INPUT_DEVICES="" declare -x INSOPTIONS="-m0644" declare IUSE="debug dist-kernel modules-sign +strip " declare -x IUSE_EFFECTIVE="abi_x86_64 alpha amd64 amd64-linux arm arm64 arm64-macos debug dist-kernel elibc_Darwin elibc_SunOS elibc_bionic elibc_glibc elibc_mingw elibc_musl hppa ia64 kernel_Darwin kernel_SunOS kernel_linux loong m68k mips modules-sign ppc ppc-macos ppc64 ppc64-linux prefix prefix-guest prefix-stack riscv s390 sparc strip x64-macos x64-solaris x86 x86-linux" declare -x IUSE_IMPLICIT="abi_x86_64 prefix prefix-guest prefix-stack" declare -x JAVAC="/etc/java-config-2/current-system-vm/bin/javac" declare -x JAVA_HOME="/etc/java-config-2/current-system-vm" declare -x JDK_HOME="/etc/java-config-2/current-system-vm" declare -x KERNEL="linux" declare -x KERNEL_ABI="amd64" declare -- KERNEL_AR="/usr/bin/x86_64-pc-linux-gnu-gcc-ar" declare -- KERNEL_CC="/usr/bin/x86_64-pc-linux-gnu-gcc-13" declare -- KERNEL_CHOST="x86_64-pc-linux-gnu" declare -- KERNEL_CXX="/usr/bin/x86_64-pc-linux-gnu-g++-13" declare -- KERNEL_DIR="/usr/src/linux" declare -- KERNEL_LD="/usr/bin/x86_64-pc-linux-gnu-ld.bfd" declare -- KERNEL_MAKEFILE="/usr/src/linux/Makefile" declare -- KERNEL_NM="/usr/bin/x86_64-pc-linux-gnu-gcc-nm" declare -- KERNEL_OBJCOPY="/usr/bin/x86_64-pc-linux-gnu-objcopy" declare -- KERNEL_OBJDUMP="/usr/bin/x86_64-pc-linux-gnu-objdump" declare -- KERNEL_READELF="/usr/bin/x86_64-pc-linux-gnu-readelf" declare -- KERNEL_STRIP="/usr/bin/x86_64-pc-linux-gnu-strip" declare -x KEYWORDS="amd64 ~arm ~arm64 ~loong ~ppc ppc64 ~riscv x86" declare -- KV_DIR="/usr/src/linux" declare -- KV_EXTRA="" declare -- KV_FULL="6.4.11-gentoo-dist" declare -- KV_LOCAL="-gentoo-dist" declare -- KV_MAJOR="6" declare -- KV_MINOR="4" declare -- KV_OUT_DIR="/usr/src/linux" declare -- KV_PATCH="11" declare -x L10N="" declare -x LANG="C.UTF8" declare -x LCD_DEVICES="" declare -x LC_COLLATE="C" declare -x LC_MESSAGES="C" declare -x LDFLAGS="-Wl,-O1 -Wl,--as-needed -Wl,--defsym=__gentoo_check_ldflags__=0" declare -x LDFLAGS_amd64="-m elf_x86_64" declare -x LDFLAGS_default declare -x LDFLAGS_x32="-m elf32_x86_64" declare -x LDFLAGS_x86="-m elf_i386" declare -x LEX="flex" declare -x LIBDIR_amd64="lib64" declare -x LIBDIR_default="lib" declare -x LIBDIR_x32="libx32" declare -x LIBDIR_x86="lib" declare -x LIBOPTIONS="-m0644" declare -x LIBREOFFICE_EXTENSIONS="" declare -x LICENSE="GPL-2" declare -x LINUX_CONFIG_EXISTS_DONE="1" declare -x LLVM_TARGETS="" declare -x LUA_SINGLE_TARGET="" declare -x LUA_TARGETS="" declare -x MAILTO="tinderbox" declare -x MAKEOPTS=" -j5" declare -x MANPAGER="manpager" declare -a MODULES_MAKEARGS=([0]="ARCH=x86" [1]="V=1" [2]="KBUILD_VERBOSE=1" [3]="CONFIG_WERROR=" [4]="CONFIG_MODULE_SIG_ALL=" [5]="CONFIG_MODULE_COMPRESS_GZIP=" [6]="CONFIG_MODULE_COMPRESS_XZ=" [7]="CONFIG_MODULE_COMPRESS_ZSTD=" [8]="DEPMOD=:" [9]="STRIP=:" [10]="CROSS_COMPILE=x86_64-pc-linux-gnu-" [11]="HOSTCC=x86_64-pc-linux-gnu-gcc" [12]="HOSTCXX=x86_64-pc-linux-gnu-g++" [13]="HOSTCFLAGS=-O2 -pipe -march=native -fno-diagnostics-color" [14]="HOSTCXXFLAGS=-O2 -pipe -march=native -fno-diagnostics-color" [15]="HOSTLDFLAGS=-Wl,-O1 -Wl,--as-needed -Wl,--defsym=__gentoo_check_ldflags__=0" [16]="HOSTPKG_CONFIG=x86_64-pc-linux-gnu-pkg-config" [17]="CC=/usr/bin/x86_64-pc-linux-gnu-gcc-13" [18]="CXX=/usr/bin/x86_64-pc-linux-gnu-g++-13" [19]="LD=/usr/bin/x86_64-pc-linux-gnu-ld.bfd" [20]="AR=/usr/bin/x86_64-pc-linux-gnu-gcc-ar" [21]="NM=/usr/bin/x86_64-pc-linux-gnu-gcc-nm" [22]="OBJCOPY=/usr/bin/x86_64-pc-linux-gnu-objcopy" [23]="OBJDUMP=/usr/bin/x86_64-pc-linux-gnu-objdump" [24]="READELF=/usr/bin/x86_64-pc-linux-gnu-readelf") declare -- MODULES_SIGN_CERT="certs/signing_key.x509" declare -x MONKEYD_PLUGINS="" declare -x MULTILIB_ABIS="amd64 x86" declare -x MULTILIB_STRICT_DENY="64-bit.*shared object" declare -x MULTILIB_STRICT_DIRS="/lib32 /lib /usr/lib32 /usr/lib /usr/kde/*/lib32 /usr/kde/*/lib /usr/qt/*/lib32 /usr/qt/*/lib /usr/X11R6/lib32 /usr/X11R6/lib" declare -x MULTILIB_STRICT_EXEMPT="(perl5|gcc|binutils|eclipse-3|debug|portage|udev|systemd|clang|python-exec|llvm)" declare -x NGINX_MODULES_HTTP="" declare -x NGINX_MODULES_MAIL="" declare -x NGINX_MODULES_STREAM="" declare -x OCAML_COLOR="never" declare -x OFFICE_IMPLEMENTATION="" declare -x OMP_DYNAMIC="FALSE" declare -x OMP_NESTED="FALSE" declare -x OMP_NUM_THREADS="5" declare -x OPENMPI_FABRICS="" declare -x OPENMPI_OFED_FEATURES="" declare -x OPENMPI_RM="" declare -x PATH="/usr/lib/portage/python3.11/ebuild-helpers/xattr:/usr/lib/portage/python3.11/ebuild-helpers:/usr/local/sbin:/usr/local/bin:/usr/sbin:/usr/bin:/sbin:/bin:/opt/bin:/usr/lib/llvm/16/bin" declare PDEPEND="" declare -x PHP_TARGETS="" declare -x PKGSYSTEM_ENABLE_FSYNC="0" declare -x PORTAGE_COMPRESSION_COMMAND="zstd -T5" declare -a PORTAGE_DOCOMPRESS=([0]="/usr/share/doc" [1]="/usr/share/info" [2]="/usr/share/man") declare -x PORTAGE_DOCOMPRESS_SIZE_LIMIT="128" declare -a PORTAGE_DOCOMPRESS_SKIP=([0]="/usr/share/doc/ovpn-dco-0.2.20230426/html") declare -a PORTAGE_DOSTRIP=([0]="/") declare -a PORTAGE_DOSTRIP_SKIP=() declare -x PORTAGE_TMPFS="/dev/shm" declare -x PORT_LOGDIR="/var/log/portage" declare -x POSTGRES_TARGETS="" declare -x PROFILE_ONLY_VARIABLES="ARCH ELIBC IUSE_IMPLICIT KERNEL USE_EXPAND_IMPLICIT USE_EXPAND_UNPREFIXED USE_EXPAND_VALUES_ARCH USE_EXPAND_VALUES_ELIBC USE_EXPAND_VALUES_KERNEL" declare -- PROPERTIES="" declare -x PYTEST_ADDOPTS="--color=no" declare -x PYTHONDONTWRITEBYTECODE="1" declare -x PYTHON_SINGLE_TARGET="" declare -x PYTHON_TARGETS="" declare -x PY_FORCE_COLOR="0" declare -x QEMU_SOFTMMU_TARGETS="" declare -x QEMU_USER_TARGETS="" declare -x QRNADB="/usr/share/qrna/data" declare RDEPEND=$'\n\tsys-apps/kmod[tools]\n\tdist-kernel? ( virtual/dist-kernel:= )\n' declare REPOSITORY declare REQUIRED_USE="" declare RESTRICT="" declare -x RESUMECOMMAND_SSH="bash -c \"x=\\\${2#ssh://} ; host=\\\${x%%/*} ; port=\\\${host##*:} ; host=\\\${host%:*} ; [[ \\\${host} = \\\${port} ]] && port= ; exec rsync --rsh=\\\"ssh \\\${port:+-p\\\${port}} \\\${3}\\\" -avP \\\"\\\${host}:/\\\${x#*/}\\\" \\\"\\\$1\\\"\" rsync \"\${DISTDIR}/\${FILE}\" \"\${URI}\" \"\${PORTAGE_SSH_OPTS}\"" declare -x ROS_MESSAGES="" declare -x RUBY_TARGETS="" declare -x RUST_TEST_TASKS="5" declare -x RUST_TEST_THREADS="5" declare -x S="/var/tmp/portage/net-vpn/ovpn-dco-0.2.20230426/work/ovpn-dco-0.2.20230426" declare -x SANDBOX_DEBUG="0" declare -x SANDBOX_DENY="" declare -x SANDBOX_METHOD="any" declare -x SANDBOX_PREDICT="/var/tmp/portage/net-vpn/ovpn-dco-0.2.20230426/homedir:/dev/crypto:/var/cache/man:/dev/random:/proc/self/coredump_filter:/dev/random:/proc/self/coredump_filter:/var/cache/fontconfig" declare -x SANDBOX_READ="/:/var/tmp/portage" declare -x SANDBOX_VERBOSE="1" declare -x SANDBOX_WRITE=":/dev/console:/dev/fd:/dev/full:/dev/null:/dev/ptmx:/dev/pts/:/dev/pty:/dev/shm:/dev/tts:/dev/tty:/dev/vc/:/dev/zero:/proc/self/fd:/tmp/:/usr/lib/cf:/usr/lib/conftest:/usr/lib32/cf:/usr/lib32/conftest:/usr/lib64/cf:/usr/lib64/conftest:/usr/tmp/:/usr/tmp/cf:/usr/tmp/conftest:/var/tmp/:/var/tmp/portage:/var/tmp/portage/net-vpn/ovpn-dco-0.2.20230426/homedir/.bash_history" declare -x SANE_BACKENDS="" declare -x SBCL_HOME="/usr/lib64/sbcl" declare -x SBCL_SOURCE_ROOT="/usr/lib64/sbcl/src" declare -x SHELL="/bin/bash" declare -- SKIP_KERNEL_CHECK="" declare -x SLOT="0" declare -i SRANDOM="473849205" declare SRC_URI="https://github.com/OpenVPN/ovpn-dco/archive/refs/tags/v0.2.20230426.tar.gz -> ovpn-dco-0.2.20230426.tar.gz" declare -x SYMLINK_LIB="no" declare -x TERMINFO="/etc/terminfo" declare -x TINDERBOX_IMAGE_NAME="17.1_desktop_plasma-20230815-141022" declare -x TWISTED_DISABLE_WRITING_OF_PLUGIN_CACHE="1" declare -x USE="abi_x86_64 amd64 elibc_glibc kernel_linux strip" declare -x USERLAND="GNU" declare -x USE_EXPAND_IMPLICIT="ARCH ELIBC KERNEL" declare -x USE_EXPAND_UNPREFIXED="ARCH" declare -x USE_EXPAND_VALUES_ARCH="alpha amd64 amd64-linux arm arm64 arm64-macos hppa ia64 loong m68k mips ppc ppc64 ppc64-linux ppc-macos riscv s390 sparc x64-macos x64-solaris x86 x86-linux" declare -x USE_EXPAND_VALUES_ELIBC="bionic Darwin glibc mingw musl SunOS" declare -x USE_EXPAND_VALUES_KERNEL="Darwin linux SunOS" declare -x UWSGI_PLUGINS="" declare -x VIDEO_CARDS="" declare -x VOICEMAIL_STORAGE="" declare -x XDG_CONFIG_DIRS="/etc/xdg" declare -x XDG_DATA_DIRS="/usr/local/share:/usr/share" declare -x XTABLES_ADDONS="" declare -x XZ_OPT="-9 -T5" declare -- _EDO_ECLASS="1" declare -- _FLAG_O_MATIC_ECLASS="1" declare -x _LINUX_CONFIG_EXISTS_DONE="1" declare -- _LINUX_INFO_ECLASS="1" declare -- _LINUX_MOD_R1_ECLASS="1" declare -A _MODULES_GLOBAL=([ran:pkg_setup]="1" ) declare -A _MODULES_INSTALL=() declare -- _MULTILIB_ECLASS="1" declare -- _MULTIPROCESSING_ECLASS="1" declare -- _TOOLCHAIN_FUNCS_ECLASS="1" declare -x __E_DESTTREE="/usr" declare -x __E_DOCDESTTREE="" declare -x __E_EXEDESTTREE="" declare -x __E_INSDESTTREE="" declare -x ac_cv_c_undeclared_builtin_options="none needed" declare -x bugz_timeout="timeout --signal=15 --kill-after=1m 3m" declare -x enable_year2038="no" declare -- get_version_warning_done="" declare -x gl_cv_compiler_check_decl_option="-Werror=implicit-function-declaration" SwitchGCC () { local highest=$(gcc-config --list-profiles --nocolor | cut -f 3 -d ' ' -s | grep -E 'x86_64-(pc|gentoo)-linux-(gnu|musl)-.*[0-9]$' | tail -n 1); if ! gcc-config --list-profiles --nocolor | grep -q -F "$highest *"; then local current=$(gcc -dumpversion); echo "major version change of gcc: $current -> $highest" | tee -a $taskfile.history; gcc-config --nocolor $highest; source_profile; add2backlog "sys-devel/libtool"; add2backlog "%emerge --unmerge sys-devel/gcc:$(cut -f 1 -d '.' <<< $current)"; fi } declare -fx SwitchGCC __eapi6_src_install () { if [[ -f Makefile || -f GNUmakefile || -f makefile ]]; then emake DESTDIR="${D}" install; fi; einstalldocs } __eapi6_src_prepare () { if ___is_indexed_array_var PATCHES; then [[ ${#PATCHES[@]} -gt 0 ]] && eapply "${PATCHES[@]}"; else if [[ -n ${PATCHES} ]]; then eapply ${PATCHES}; fi; fi; eapply_user } __eapi7_ver_compare () { local va=${1} vb=${2} a an al as ar b bn bl bs br re LC_ALL=C; re="^([0-9]+(\.[0-9]+)*)([a-z]?)((_(alpha|beta|pre|rc|p)[0-9]*)*)(-r[0-9]+)?$"; [[ ${va} =~ ${re} ]] || die "${FUNCNAME}: invalid version: ${va}"; an=${BASH_REMATCH[1]}; al=${BASH_REMATCH[3]}; as=${BASH_REMATCH[4]}; ar=${BASH_REMATCH[7]}; [[ ${vb} =~ ${re} ]] || die "${FUNCNAME}: invalid version: ${vb}"; bn=${BASH_REMATCH[1]}; bl=${BASH_REMATCH[3]}; bs=${BASH_REMATCH[4]}; br=${BASH_REMATCH[7]}; __eapi7_ver_compare_int "${an%%.*}" "${bn%%.*}" || return; while [[ ${an} == *.* && ${bn} == *.* ]]; do an=${an#*.}; bn=${bn#*.}; a=${an%%.*}; b=${bn%%.*}; if [[ ${a} == 0* || ${b} == 0* ]]; then [[ ${a} =~ 0+$ ]] && a=${a%"${BASH_REMATCH[0]}"}; [[ ${b} =~ 0+$ ]] && b=${b%"${BASH_REMATCH[0]}"}; [[ ${a} > ${b} ]] && return 3; [[ ${a} < ${b} ]] && return 1; else __eapi7_ver_compare_int "${a}" "${b}" || return; fi; done; [[ ${an} == *.* ]] && return 3; [[ ${bn} == *.* ]] && return 1; [[ ${al} > ${bl} ]] && return 3; [[ ${al} < ${bl} ]] && return 1; as=${as#_}${as:+_}; bs=${bs#_}${bs:+_}; while [[ -n ${as} && -n ${bs} ]]; do a=${as%%_*}; b=${bs%%_*}; if [[ ${a%%[0-9]*} == "${b%%[0-9]*}" ]]; then __eapi7_ver_compare_int "${a##*[a-z]}" "${b##*[a-z]}" || return; else [[ ${a%%[0-9]*} == p ]] && return 3; [[ ${b%%[0-9]*} == p ]] && return 1; [[ ${a} > ${b} ]] && return 3 || return 1; fi; as=${as#*_}; bs=${bs#*_}; done; if [[ -n ${as} ]]; then [[ ${as} == p[_0-9]* ]] && return 3 || return 1; else if [[ -n ${bs} ]]; then [[ ${bs} == p[_0-9]* ]] && return 1 || return 3; fi; fi; __eapi7_ver_compare_int "${ar#-r}" "${br#-r}" || return; return 2 } __eapi7_ver_compare_int () { local a=$1 b=$2 d=$(( ${#1}-${#2} )); if [[ ${d} -gt 0 ]]; then printf -v b "%0${d}d%s" 0 "${b}"; else if [[ ${d} -lt 0 ]]; then printf -v a "%0$(( -d ))d%s" 0 "${a}"; fi; fi; [[ ${a} > ${b} ]] && return 3; [[ ${a} == "${b}" ]] } __eapi7_ver_parse_range () { local range=${1}; local max=${2}; [[ ${range} == [0-9]* ]] || die "${FUNCNAME}: range must start with a number"; start=${range%-*}; [[ ${range} == *-* ]] && end=${range#*-} || end=${start}; if [[ -n ${end} ]]; then [[ ${start} -le ${end} ]] || die "${FUNCNAME}: end of range must be >= start"; [[ ${end} -le ${max} ]] || end=${max}; else end=${max}; fi } __eapi7_ver_split () { local v=${1} LC_ALL=C; comp=(); local s c; while [[ -n ${v} ]]; do s=${v%%[a-zA-Z0-9]*}; v=${v:${#s}}; [[ ${v} == [0-9]* ]] && c=${v%%[^0-9]*} || c=${v%%[^a-zA-Z]*}; v=${v:${#c}}; comp+=("${s}" "${c}"); done } __eapi8_src_prepare () { local f; if ___is_indexed_array_var PATCHES; then [[ ${#PATCHES[@]} -gt 0 ]] && eapply -- "${PATCHES[@]}"; else if [[ -n ${PATCHES} ]]; then eapply -- ${PATCHES}; fi; fi; eapply_user } _clang_fullversion () { local ver="$1"; shift; set -- $($(tc-getCPP "$@") -E -P - <<< "__clang_major__ __clang_minor__ __clang_patchlevel__"); eval echo "${ver}" } _filter-hardened () { local f; for f in "$@"; do case "${f}" in -fPIC | -fpic | -fPIE | -fpie | -Wl,pie | -pie) gcc-specs-pie || continue; if ! is-flagq -nopie && ! is-flagq -no-pie; then if test-flags -nopie > /dev/null; then append-flags -nopie; else append-flags -no-pie; fi; fi ;; -fstack-protector) gcc-specs-ssp || continue; is-flagq -fno-stack-protector || append-flags $(test-flags -fno-stack-protector) ;; -fstack-protector-all) gcc-specs-ssp-to-all || continue; is-flagq -fno-stack-protector-all || append-flags $(test-flags -fno-stack-protector-all) ;; -fno-strict-overflow) gcc-specs-nostrict || continue; is-flagq -fstrict-overflow || append-flags $(test-flags -fstrict-overflow) ;; esac; done } _filter-var () { local f x var=$1 new=(); shift; for f in ${!var}; do for x in "$@"; do [[ ${f} == ${x} ]] && continue 2; done; new+=("${f}"); done; export ${var}="${new[*]}" } _gcc-install-dir () { echo "$(LC_ALL=C $(tc-getCC) -print-search-dirs 2> /dev/null | awk '$1=="install:" {print $2}')" } _gcc-specs-directive_raw () { local cc=$(tc-getCC); local specfiles=$(LC_ALL=C ${cc} -v 2>&1 | awk '$1=="Reading" {print $NF}'); ${cc} -dumpspecs 2> /dev/null | cat - ${specfiles} | awk -v directive=$1 'BEGIN { pspec=""; spec=""; outside=1 } $1=="*"directive":" { pspec=spec; spec=""; outside=0; next } outside || NF==0 || ( substr($1,1,1)=="*" && substr($1,length($1),1)==":" ) { outside=1; next } spec=="" && substr($0,1,1)=="+" { spec=pspec " " substr($0,2); next } { spec=spec $0 } END { print spec }'; return 0 } _gcc-specs-exists () { [[ -f $(_gcc-install-dir)/$1 ]] } _gcc_fullversion () { local ver="$1"; shift; set -- $($(tc-getCPP "$@") -E -P - <<< "__GNUC__ __GNUC_MINOR__ __GNUC_PATCHLEVEL__"); eval echo "${ver}" } _is_flagq () { local x var="$1[*]"; for x in ${!var}; do [[ ${x} == $2 ]] && return 0; done; return 1 } _modules_check_function () { [[ -z ${MODULES_OPTIONAL_IUSE} ]] || use "${MODULES_OPTIONAL_IUSE#+}" || return 1; [[ ${#} == 0 || ${1} -ge ${2} && ( ! -n ${3} || ${1} -le ${3} ) ]] || die "Usage: ${FUNCNAME[1]} ${4-(no arguments)}"; [[ -v _MODULES_GLOBAL[ran:pkg_setup] ]] || die "${FUNCNAME[1]} was called without running linux-mod-r1_pkg_setup" } _modules_check_migration () { function _modules_check_var () { [[ -z ${!1} ]] || die "${1} is obsolete, see ${2} in linux-mod-r1 eclass docs" }; _modules_check_var MODULES_OPTIONAL_USE MODULES_OPTIONAL_IUSE; _modules_check_var MODULES_OPTIONAL_USE_IUSE_DEFAULT MODULES_OPTIONAL_IUSE; _modules_check_var BUILD_PARAMS modargs; _modules_check_var BUILD_TARGETS modlist; _modules_check_var MODULE_NAMES modlist; [[ -z ${!MODULESD_*} ]] || die "MODULESD_* variables are no longer supported, replace by handcrafted .conf files if needed" } _modules_check_var () { [[ -z ${!1} ]] || die "${1} is obsolete, see ${2} in linux-mod-r1 eclass docs" } _modules_prepare_kernel () { get_version; [[ -n ${KV_FULL} ]] || die "kernel sources are required to build kernel modules"; require_configured_kernel; _modules_sanity_kernelbuilt; _modules_sanity_kernelversion; local CONFIG_CHECK="${CONFIG_CHECK} MODULES"; if [[ $(linux_chkconfig_string UNUSED_KSYMS_WHITELIST) == \"+(?)\" ]]; then CONFIG_CHECK+=" ~!TRIM_UNUSED_KSYMS"; else CONFIG_CHECK+=" !TRIM_UNUSED_KSYMS"; fi; linux-info_pkg_setup } _modules_prepare_sign () { use modules-sign || return 0; function _modules_sign_die () { eerror "USE=modules-sign requires additional configuration, please see the"; eerror "kernel[1] documentation and the linux-mod-r1 eclass[2] user variables."; eerror "[1] https://www.kernel.org/doc/html/v${KV_MAJOR}.${KV_MINOR}/admin-guide/module-signing.html"; eerror "[2] https://devmanual.gentoo.org/eclass-reference/linux-mod-r1.eclass/index.html"; die "USE=modules-sign is set but ${*}" }; linux_chkconfig_present MODULE_SIG || _modules_sign_die "CONFIG_MODULE_SIG is not set in the kernel"; if [[ -z ${MODULES_SIGN_HASH} ]]; then : "$(linux_chkconfig_string MODULE_SIG_HASH)"; MODULES_SIGN_HASH=${_//\"}; [[ -n ${MODULES_SIGN_HASH} ]] || _modules_sign_die "CONFIG_MODULE_SIG_HASH is not set in the kernel"; fi; if [[ -z ${MODULES_SIGN_KEY} ]]; then : "$(linux_chkconfig_string MODULE_SIG_KEY)"; MODULES_SIGN_KEY=${_//\"}; [[ -n ${MODULES_SIGN_KEY} ]] || _modules_sign_die "CONFIG_MODULE_SIG_KEY is not set in the kernel"; fi; [[ ${MODULES_SIGN_KEY} != @(/|pkcs11:)* ]] && MODULES_SIGN_KEY=${KV_OUT_DIR}/${MODULES_SIGN_KEY}; [[ ${MODULES_SIGN_CERT} != /* ]] && MODULES_SIGN_CERT=${KV_OUT_DIR}/${MODULES_SIGN_CERT}; [[ ${MODULES_SIGN_KEY} == pkcs11:* || -f ${MODULES_SIGN_KEY} ]] || _modules_sign_die "the private key '${MODULES_SIGN_KEY}' was not found"; [[ -f ${MODULES_SIGN_CERT} ]] || _modules_sign_die "the public key certificate '${MODULES_SIGN_CERT}' was not found" } _modules_prepare_toolchain () { [[ -z ${KERNEL_CHOST} ]] && linux_chkconfig_present 64BIT && case ${CHOST} in hppa2.0-*) KERNEL_CHOST=${CHOST/2.0/64} ;; esac; : "${KERNEL_CHOST:=${CHOST}}"; einfo "Preparing ${KERNEL_CHOST} toolchain for kernel modules (override with KERNEL_CHOST) ..."; function _modules_tc_best () { [[ -z ${!1} ]] && read -r ${1} < <(type -P -- "${@:2}") }; local gccv clangv tool; if linux_chkconfig_present CC_IS_GCC; then gccv=$(linux_chkconfig_string GCC_VERSION); gccv=${gccv::2}; _modules_tc_best KERNEL_CC {"${KERNEL_CHOST}-",}gcc{"-${gccv}",}; _modules_tc_best KERNEL_CXX {"${KERNEL_CHOST}-",}g++{"-${gccv}",}; for tool in AR NM OBJCOPY OBJDUMP READELF STRIP; do _modules_tc_best KERNEL_${tool} {"${KERNEL_CHOST}-",}{gcc-,}${tool,,}; done; else if linux_chkconfig_present CC_IS_CLANG; then clangv=$(linux_chkconfig_string CLANG_VERSION); clangv=${clangv::2}; _modules_tc_best KERNEL_CC {"${BROOT}/usr/lib/llvm/${clangv}/bin/",}{"${KERNEL_CHOST}-",}clang{"-${clangv}",}; _modules_tc_best KERNEL_CXX {"${BROOT}/usr/lib/llvm/${clangv}/bin/",}{"${KERNEL_CHOST}-",}clang++{"-${clangv}",}; for tool in AR NM OBJCOPY OBJDUMP READELF STRIP; do _modules_tc_best KERNEL_${tool} {"${BROOT}/usr/lib/llvm/${clangv}/bin/",}{"${KERNEL_CHOST}-",}{llvm-,}${tool,,}; done; fi; fi; if linux_chkconfig_present LD_IS_BFD; then _modules_tc_best KERNEL_LD {"${KERNEL_CHOST}-",}ld.bfd; else if linux_chkconfig_present LD_IS_LLD; then _modules_tc_best KERNEL_LD {${clangv+"${BROOT}/usr/lib/llvm/${clangv}/bin/"},}{"${KERNEL_CHOST}-",}ld.lld; fi; fi; local CHOST=${KERNEL_CHOST}; : "${KERNEL_CC:=$(tc-getCC)}"; : "${KERNEL_CXX:=$(tc-getCXX)}"; : "${KERNEL_LD:=$(tc-getLD)}"; : "${KERNEL_AR:=$(tc-getAR)}"; : "${KERNEL_NM:=$(tc-getNM)}"; : "${KERNEL_OBJCOPY:=$(tc-getOBJCOPY)}"; : "${KERNEL_OBJDUMP:=$(tc-getOBJDUMP)}"; : "${KERNEL_READELF:=$(tc-getREADELF)}"; : "${KERNEL_STRIP:=$(tc-getSTRIP)}"; local CC=${KERNEL_CC} CPP="${KERNEL_CC} -E" LD=${KERNEL_LD}; einfo "Toolchain picked for kernel modules (override with KERNEL_CC, _LD, ...):" "'${KERNEL_CC}' '${KERNEL_CXX}' '${KERNEL_LD}' '${KERNEL_AR}'" "'${KERNEL_NM}' '${KERNEL_OBJCOPY}' '${KERNEL_OBJDUMP}'" "'${KERNEL_READELF}' '${KERNEL_STRIP}'"; if linux_chkconfig_present LTO_CLANG_THIN && tc-ld-is-lld; then KERNEL_LD=${T}/linux-mod-r1_ld.lld; printf '#!/usr/bin/env sh\nexec %s "${@}" --thinlto-cache-dir=\n' "${LD}" > "${KERNEL_LD}" || die; chmod +x -- "${KERNEL_LD}" || die; fi; local warn; if [[ -v gccv ]]; then if ! tc-is-gcc; then warn="gcc-${gccv} but\n '${KERNEL_CC}' is not gcc"; else if [[ $(gcc-major-version) -ne "${gccv}" ]]; then warn="gcc-${gccv} but\n '${KERNEL_CC}' is gcc-$(gcc-major-version)"; fi; fi; else if [[ -v clangv ]]; then if ! tc-is-clang; then warn="clang-${clangv} but\n '${KERNEL_CC}' is not clang"; else if [[ $(clang-major-version) -ne "${clangv}" ]]; then warn="clang-${clangv} but\n '${KERNEL_CC}' is clang-$(clang-major-version)"; fi; fi; fi; fi; if [[ -v warn ]]; then ewarn; ewarn "Warning: kernel ${KV_FULL} is built with ${warn}"; ewarn "This *could* result in build issues or other incompatibilities."; ewarn "It is recommended to either \`make clean\` and rebuild the kernel"; ewarn "with the current toolchain (for distribution kernels, re-installing"; ewarn "will do the same), or set the KERNEL_CC variable to point to the"; ewarn "same compiler. Note that when it is available, auto-selection is"; ewarn "attempted making the latter rarely needed."; ewarn; fi } _modules_process_compress () { local -a compress; if linux_chkconfig_present MODULE_COMPRESS_XZ; then compress=(xz -qT"$(makeopts_jobs)" --memlimit-compress=50%); else if linux_chkconfig_present MODULE_COMPRESS_GZIP; then if type -P pigz &> /dev/null; then compress=(pigz -p"$(makeopts_jobs)"); else compress=(gzip); fi; else if linux_chkconfig_present MODULE_COMPRESS_ZSTD; then compress=(zstd -qT"$(makeopts_jobs)" --rm); fi; fi; fi; if [[ -v compress ]]; then einfo "Compressing modules (matching the kernel configuration) ..."; edob "${compress[@]}" -- "${@}"; fi } _modules_process_depmod.d () { ( [[ ${SLOT%/*} == 0 ]] && slot= || slot=-${SLOT%/*}; insinto /lib/depmod.d; newins - ${PN}${slot}.conf < <(echo "# Automatically generated by linux-mod-r1.eclass for ${CATEGORY}/${PN}" for mod in "$@"; do [[ ${mod} =~ ^(.+)/(.+).ko$ ]] && echo "override ${BASH_REMATCH[2]} ${KV_FULL} ${BASH_REMATCH[1]}"; done) ) } _modules_process_sign () { use modules-sign || return 0; local sign=; if [[ -f ${KV_DIR}/scripts/sign-file.c ]]; then sign=${T}/linux-mod-r1_sign-file; ( einfo "Compiling sign-file ..."; tc-export_build_env; nonfatal edob $(tc-getBUILD_CC) ${BUILD_CFLAGS} ${BUILD_CPPFLAGS} $($(tc-getBUILD_PKG_CONFIG) --cflags libcrypto) ${BUILD_LDFLAGS} -o "${sign}" "${KV_DIR}"/scripts/sign-file.c $($(tc-getBUILD_PKG_CONFIG) --libs libcrypto || echo -lcrypto) ) || { einfo "Trying fallback ..."; sign= }; fi; if [[ -z ${sign} ]]; then if [[ -x ${KV_OUT_DIR}/scripts/sign-file ]]; then sign=${KV_OUT_DIR}/scripts/sign-file; else if [[ -x ${KV_DIR}/scripts/sign-file ]]; then sign=${KV_DIR}/scripts/sign-file; else die "USE=modules-sign is set but '${KV_DIR}/scripts/sign-file.c' is not usable"; fi; fi; fi; einfo "Signing modules ..."; [[ ${MODULES_SIGN_KEY} == pkcs11:* || -r ${MODULES_SIGN_KEY} ]] || die "USE=modules-sign is set but lacking read access to the signing key at '${MODULES_SIGN_KEY}'"; local mod; for mod in "$@"; do edob "${sign}" "${MODULES_SIGN_HASH}" "${MODULES_SIGN_KEY}" "${MODULES_SIGN_CERT}" "${mod}"; done; unset KBUILD_SIGN_PIN } _modules_process_strip () { dostrip -x "${@#"${ED}"}"; if use strip; then einfo "Stripping modules ..."; edob "${KERNEL_STRIP}" --strip-unneeded -- "${@}"; fi } _modules_sanity_gccplugins () { linux_chkconfig_present GCC_PLUGINS || return 0; local tmp=${T}/linux-mod-r1_gccplugins; mkdir -p -- "${tmp}" || die; echo "obj-m += test.o" > "${tmp}"/Kbuild || die; : > "${tmp}"/test.c || die; local output=$(cd -- "${KV_OUT_DIR}" && LC_ALL=C nonfatal emake "${MODULES_MAKEARGS[@]}" M="${tmp}" 2>&1 > /dev/null); if [[ ${output} == *"error: incompatible gcc/plugin version"* ]]; then eerror "GCC_PLUGINS is enabled in the kernel and plugin version mismatch issues"; eerror "have been detected. Please \`make clean\` and rebuild the kernel using"; eerror "the current version of GCC (or re-install for distribution kernels)."; die "kernel ${KV_FULL} needs to be rebuilt"; fi } _modules_sanity_kernelbuilt () { local symvers=${KV_OUT_DIR}/Module.symvers; if [[ ! -f ${symvers} ]]; then eerror "'${symvers}' was not found implying that the"; eerror "linux-${KV_FULL} tree at that location has not been built."; eerror; eerror "Please verify that this is the intended kernel version, then perform"; eerror "a full build[1] (i.e. make && make modules_install && make install)."; eerror; eerror "Alternatively, consider a distribution kernel[2] that does not need"; eerror "these manual steps (e.g. sys-kernel/gentoo-kernel or gentoo-kernel-bin)."; eerror; eerror "[1] https://wiki.gentoo.org/wiki/Kernel/Configuration#Build"; eerror "[2] https://wiki.gentoo.org/wiki/Project:Distribution_Kernel"; die "built kernel sources are required to build kernel modules"; fi; if [[ ! -r ${symvers} ]]; then eerror "'${symvers}' exists but cannot be read by the"; eerror "user id(${EUID}) of the package manager, likely implying no world"; eerror "read access permissions:"; eerror; eerror " $(ls -l -- "${symvers}")"; eerror; eerror "Causes may vary, but a common one is building the kernel with a umask"; eerror "value of '0077' rather than the more typical '0022' (run the \`umask\`"; eerror "command to confirm, as root if was building the kernel using it)."; eerror; eerror "Many other files are likely affected and will lead to build failures."; eerror "It is recommended to clean the sources and rebuild with \`umask 0022\`"; eerror "rather than attempt to fix the permissions manually."; die "no read access permission to the generated kernel files"; fi } _modules_sanity_kernelversion () { local kv=${KV_MAJOR}.${KV_MINOR}.${KV_PATCH}; if [[ -n ${MODULES_KERNEL_MIN} ]] && ver_test "${kv}" -lt "${MODULES_KERNEL_MIN}"; then eerror "${P} requires a kernel version of at least >=${MODULES_KERNEL_MIN},"; eerror "but the current kernel is ${KV_FULL}. Please update."; die "kernel ${KV_FULL} is too old"; fi; if [[ -n ${MODULES_KERNEL_MAX} ]]; then : "${MODULES_KERNEL_MAX//[^.]/}"; local -i count=${#_}; if ver_test "$(ver_cut 1-$((count+1)) "${kv}")" -gt "${MODULES_KERNEL_MAX}"; then local max=${MODULES_KERNEL_MAX}; [[ ${count} -lt 2 ]] && max+=.x; ewarn; ewarn " *** WARNING *** "; ewarn; ewarn "${PN} is known to break easily with new kernel versions and,"; ewarn "with the current kernel (${KV_FULL}), it was either hardly"; ewarn "tested or is known broken. It is recommended to use one of:"; ewarn; if use dist-kernel; then ewarn " <=virtual/dist-kernel-${max} or"; else ewarn " <=sys-kernel/gentoo-kernel-${max} or"; fi; ewarn " <=sys-kernel/gentoo-sources-${max}"; ewarn; ewarn "or equivalent rather than file downstream bug reports if run into"; ewarn "issues, then wait for upstream fixes and a new release. Ideally,"; ewarn "with out-of-tree modules, use an LTS (Long Term Support) kernel"; ewarn "branch[1]. If in doubt, Gentoo's stable kernels are always LTS"; ewarn "and can be easily used even on ~testing systems."; ewarn; ewarn "[1] https://www.kernel.org/category/releases.html"; ewarn; fi; fi } _modules_sanity_modversion () { local mod ver; for mod in "$@"; do read -rd ' ' ver < <(LC_ALL=C modinfo -F vermagic -- "${mod}" || die "modinfo failed to read module '${mod}' (broken module?)"); [[ -n ${ver} ]] || die "modinfo found no kernel version in '${mod}' (broken module?)"; if [[ ${ver} != "${KV_FULL}" ]]; then eerror "A module seem to have been built for kernel version '${ver}'"; eerror "while it was meant for '${KV_FULL}'. This may indicate an"; eerror "ebuild issue (e.g. used runtime \`uname -r\` kernel rather than"; eerror "the chosen sources). Please report this to the ebuild's maintainer."; die "module and source version mismatch in '${mod}'"; fi; done } _modules_set_makeargs () { MODULES_MAKEARGS=(ARCH="$(tc-arch-kernel)" V=1 KBUILD_VERBOSE=1 CONFIG_WERROR= CONFIG_MODULE_{SIG_ALL,COMPRESS_{GZIP,XZ,ZSTD}}= DEPMOD=: STRIP=:); if [[ ! -n ${MODULES_I_WANT_FULL_CONTROL} ]]; then MODULES_MAKEARGS+=(CROSS_COMPILE="${KERNEL_CHOST}-" HOSTCC="$(tc-getBUILD_CC)" HOSTCXX="$(tc-getBUILD_CXX)" HOSTCFLAGS="$(tc-export_build_env; echo "${BUILD_CFLAGS}")" HOSTCXXFLAGS="$(tc-export_build_env; echo "${BUILD_CXXFLAGS}")" HOSTLDFLAGS="$(tc-export_build_env; echo "${BUILD_LDFLAGS}")" HOSTPKG_CONFIG="$(tc-getBUILD_PKG_CONFIG)" CC="${KERNEL_CC}" CXX="${KERNEL_CXX}" LD="${KERNEL_LD}" AR="${KERNEL_AR}" NM="${KERNEL_NM}" OBJCOPY="${KERNEL_OBJCOPY}" OBJDUMP="${KERNEL_OBJDUMP}" READELF="${KERNEL_READELF}"); fi; eval "MODULES_MAKEARGS+=( ${MODULES_EXTRA_EMAKE} )" || die } _modules_tc_best () { [[ -z ${!1} ]] && read -r ${1} < <(type -P -- "${@:2}") } _modules_update_depmod () { local map=${EROOT}/lib/modules/${KV_FULL}/build/System.map; if [[ ! -f ${map} ]]; then map=${KV_OUT_DIR}/System.map; [[ ! -f ${map} ]] && map=${EROOT}/boot/System.map-${KV_FULL}; fi; einfo "Updating module dependencies for kernel ${KV_FULL} ..."; if [[ -f ${map} ]]; then local depmodargs=(-ae -F "${map}" "${KV_FULL}"); [[ -n ${EROOT} ]] && depmodargs+=(-b "${EROOT}" --config="${EROOT}"/{etc,run,usr/local/lib,lib}/depmod.d); nonfatal edob depmod "${depmodargs[@]}" && return 0; else eerror; eerror "System.map for kernel ${KV_FULL} was not found, may be due to the"; eerror "built kernel sources no longer being available and lacking the fallback:"; eerror; eerror "${EROOT}/boot/System.map-${KV_FULL}"; fi; eerror; eerror "Some modules may not load without updating manually using depmod." } _setup-allowed-flags () { ALLOWED_FLAGS=(-pipe -O '-O[123szg]' '-mcpu=*' '-march=*' '-mtune=*' -flto '-flto=*' -fno-lto '-fstack-protector*' -fstack-clash-protection '-fcf-protection=*' -fbounds-check -fbounds-checking -fno-PIE -fno-pie -nopie -no-pie '-mindirect-branch=*' -mindirect-branch-register '-mfunction-return=*' -mretpoline -fno-unit-at-a-time -fno-strict-overflow '-fsanitize*' '-fno-sanitize*' -g '-g[0-9]' -ggdb '-ggdb[0-9]' -gdwarf '-gdwarf-*' -gstabs -gstabs+ -gz -glldb -fno-diagnostics-color '-fmessage-length=*' -fno-ident -fpermissive -frecord-gcc-switches -frecord-command-line '-fdiagnostics*' '-fplugin*' '-W*' -w '-[DUILR]*' '-Wl,*' '-fuse-ld=*'); ALLOWED_FLAGS+=('-fno-stack-protector*' '-fabi-version=*' -fno-strict-aliasing -fno-bounds-check -fno-bounds-checking -fstrict-overflow -fno-omit-frame-pointer '-fno-builtin*'); ALLOWED_FLAGS+=('-mregparm=*' -mno-app-regs -mapp-regs -mno-mmx -mno-sse -mno-sse2 -mno-sse3 -mno-ssse3 -mno-sse4 -mno-sse4.1 -mno-sse4.2 -mno-avx -mno-aes -mno-pclmul -mno-sse4a -mno-3dnow -mno-popcnt -mno-abm -mips1 -mips2 -mips3 -mips4 -mips32 -mips64 -mips16 -mplt -msoft-float -mno-soft-float -mhard-float -mno-hard-float '-mfpu=*' -mieee -mieee-with-inexact '-mschedule=*' -mfloat-gprs -mspe -mno-spe -mtls-direct-seg-refs -mno-tls-direct-seg-refs -mflat -mno-flat -mno-faster-structs -mfaster-structs -m32 -m64 -mx32 '-mabi=*' -mlittle-endian -mbig-endian -EL -EB -fPIC -mlive-g0 '-mcmodel=*' -mstack-bias -mno-stack-bias -msecure-plt '-m*-toc' '-mfloat-abi=*' -mfix-r4000 -mno-fix-r4000 -mfix-r4400 -mno-fix-r4400 -mfix-rm7000 -mno-fix-rm7000 -mfix-r10000 -mno-fix-r10000 '-mr10k-cache-barrier=*' -mthumb -marm -ffixed-x18 -mno-fma4 -mno-movbe -mno-xop -mno-lwp -mno-fsgsbase -mno-rdrnd -mno-f16c -mno-bmi -mno-tbm -mno-avx2 -mno-bmi2 -mno-fma -mno-lzcnt -mno-fxsr -mno-hle -mno-rtm -mno-xsave -mno-xsaveopt -mno-avx512cd -mno-avx512er -mno-avx512f -mno-avx512pf -mno-sha); ALLOWED_FLAGS+=(-mstackrealign) } _tc-getPROG () { local tuple=$1; local v var vars=$2; local prog=($3); var=${vars%% *}; for v in ${vars}; do if [[ -n ${!v} ]]; then export ${var}="${!v}"; echo "${!v}"; return 0; fi; done; local search=; [[ -n $4 ]] && search=$(type -p $4-${prog[0]}); [[ -z ${search} && -n ${!tuple} ]] && search=$(type -p ${!tuple}-${prog[0]}); [[ -n ${search} ]] && prog[0]=${search##*/}; export ${var}="${prog[*]}"; echo "${!var}" } _tc-has-openmp () { local base="${T}/test-tc-openmp"; cat <<-EOF > "${base}.c" #include int main(void) { int nthreads, tid, ret = 0; #pragma omp parallel private(nthreads, tid) { tid = omp_get_thread_num(); nthreads = omp_get_num_threads(); ret += tid + nthreads; } return ret; } EOF $(tc-getCC "$@") -fopenmp "${base}.c" -o "${base}" >&/dev/null; local ret=$?; rm -f "${base}"*; return ${ret} } _test-flag-PROG () { local comp=$1; local lang=$2; shift 2; if [[ -z ${comp} ]]; then return 1; fi; if [[ -z $1 ]]; then return 1; fi; comp=($(tc-get${comp})); if ! type -p ${comp[0]} > /dev/null; then return 1; fi; local in_src in_ext cmdline_extra=(); case "${lang}" in c) in_ext='c'; in_src='int main(void) { return 0; }'; cmdline_extra+=(-xc -c) ;; c++) in_ext='cc'; in_src='int main(void) { return 0; }'; cmdline_extra+=(-xc++ -c) ;; f77) in_ext='f'; in_src=' end'; cmdline_extra+=(-xf77 -c) ;; f95) in_ext='f90'; in_src='end'; cmdline_extra+=(-xf95 -c) ;; c+ld) in_ext='c'; in_src='int main(void) { return 0; }'; if is-ldflagq -fuse-ld=*; then fuse_ld_value=$(get-flag -fuse-ld=*); cmdline_extra+=(${fuse_ld_value}); fi; cmdline_extra+=(-xc) ;; esac; local test_in=${T}/test-flag.${in_ext}; local test_out=${T}/test-flag.exe; printf "%s\n" "${in_src}" > "${test_in}" || die "Failed to create '${test_in}'"; local cmdline=("${comp[@]}" -Werror "$@" "${cmdline_extra[@]}" "${test_in}" -o "${test_out}"); "${cmdline[@]}" &> /dev/null } _test-flags-PROG () { local comp=$1; local flags=(); local x; shift; [[ -z ${comp} ]] && return 1; while (( $# )); do case "$1" in --param | -B) if test-flag-${comp} "$1" "$2"; then flags+=("$1" "$2"); fi; shift 2 ;; *) if test-flag-${comp} "$1"; then flags+=("$1"); fi; shift 1 ;; esac; done; echo "${flags[*]}"; [[ ${#flags[@]} -gt 0 ]] } add2backlog () { local bl=/var/tmp/tb/backlog.1st; if [[ $1 == '@preserved-rebuild' ]]; then sed -i -e "/@preserved-rebuild/d" $bl; sed -i -e "1 i\@preserved-rebuild" $bl; return; fi; if [[ $1 =~ ^@ || $1 =~ ^% ]]; then if [[ "$(tail -n 1 $bl)" != "$1" ]]; then echo "$1" >> $bl; fi; else if ! grep -q "^${1}$" $bl; then echo "$1" >> $bl; fi; fi } declare -fx add2backlog all-flag-vars () { echo {ADA,C,CPP,CXX,CCAS,F,FC,LD}FLAGS } append-atomic-flags () { local code; read -r -d '' code <<-EOF int main(void) { return 0; } EOF test-compile "c+ld" "${code}" || return; local bytesizes; [[ "${#}" == "0" ]] && bytesizes=("1" "2" "4" "8") || bytesizes="${@}"; for bytesize in ${bytesizes[@]}; do read -r -d '' code <<-EOF #include int main(void) { uint$((${bytesize} * 8))_t a = 0; __atomic_add_fetch(&a, 3, __ATOMIC_RELAXED); __atomic_compare_exchange_n(&a, &a, 2, 1, __ATOMIC_RELAXED, __ATOMIC_RELAXED); return 0; } EOF test-compile "c+ld" "${code}" && continue test-flags-CCLD "-latomic" &> /dev/null || die "-latomic is required but not supported by $(tc-getCC)"; append-libs "-latomic"; test-compile "c+ld" "${code}" || die "libatomic does not include an implementation of ${bytesize}-byte atomics for this toolchain"; return; done } append-cflags () { [[ $# -eq 0 ]] && return 0; export CFLAGS+=" $*"; return 0 } append-cppflags () { [[ $# -eq 0 ]] && return 0; export CPPFLAGS+=" $*"; return 0 } append-cxxflags () { [[ $# -eq 0 ]] && return 0; export CXXFLAGS+=" $*"; return 0 } append-fflags () { [[ $# -eq 0 ]] && return 0; export FFLAGS+=" $*"; export FCFLAGS+=" $*"; return 0 } append-flags () { [[ $# -eq 0 ]] && return 0; case " $* " in *' '-[DIU]*) eqawarn 'Please use append-cppflags for preprocessor flags' ;; *' '-L* | *' '-Wl,*) eqawarn 'Please use append-ldflags for linker flags' ;; esac; append-cflags "$@"; append-cxxflags "$@"; append-fflags "$@"; return 0 } append-ldflags () { [[ $# -eq 0 ]] && return 0; local flag; for flag in "$@"; do [[ ${flag} == -l* ]] && eqawarn "Appending a library link instruction (${flag}); libraries to link to should not be passed through LDFLAGS"; done; export LDFLAGS="${LDFLAGS} $*"; return 0 } append-lfs-flags () { [[ $# -ne 0 ]] && die "append-lfs-flags takes no arguments"; append-cppflags -D_FILE_OFFSET_BITS=64 -D_LARGEFILE_SOURCE -D_LARGEFILE64_SOURCE } append-libs () { [[ $# -eq 0 ]] && return 0; local flag; for flag in "$@"; do if [[ -z "${flag// }" ]]; then eqawarn "Appending an empty argument to LIBS is invalid! Skipping."; continue; fi; case $flag in -[lL]*) export LIBS="${LIBS} ${flag}" ;; -*) eqawarn "Appending non-library to LIBS (${flag}); Other linker flags should be passed via LDFLAGS"; export LIBS="${LIBS} ${flag}" ;; *) export LIBS="${LIBS} -l${flag}" ;; esac; done; return 0 } check_extra_config () { use kernel_linux || return; local config negate die error reworkmodulenames; local soft_errors_count=0 hard_errors_count=0 config_required=0; local old_LINUX_CONFIG_EXISTS_DONE="${_LINUX_CONFIG_EXISTS_DONE}"; linux-info_get_any_version; for config in ${CONFIG_CHECK}; do if [[ "${config:0:1}" != "~" ]]; then config_required=1; break; fi; done; if [[ ${config_required} == 0 ]]; then if ! linux_config_exists; then ewarn "Unable to check for the following kernel config options due"; ewarn "to absence of any configured kernel sources or compiled"; ewarn "config:"; for config in ${CONFIG_CHECK}; do config=${config#\~}; config=${config#\!}; local_error="ERROR_${config}"; msg="${!local_error}"; if [[ -z ${msg} ]]; then local_error="WARNING_${config}"; msg="${!local_error}"; fi; ewarn " - ${config}${msg:+ - }${msg}"; done; ewarn "You're on your own to make sure they are set if needed."; export LINUX_CONFIG_EXISTS_DONE="${old_LINUX_CONFIG_EXISTS_DONE}"; return 0; fi; else if ! linux_config_exists; then qeerror "Could not find a neither a usable .config in the kernel source directory"; qeerror "nor a /proc/config.gz file,"; qeerror "Please ensure that ${KERNEL_DIR} points to a configured set of Linux sources."; qeerror "If you are using KBUILD_OUTPUT, please set the environment var so that"; qeerror "it points to the necessary object directory so that it might find .config"; qeerror "or have a properly configured kernel to produce a config.gz file. (CONFIG_IKCONFIG)."; die "Kernel not configured; no .config found in ${KV_OUT_DIR} or /proc/config.gz found"; fi; fi; ebegin "Checking for suitable kernel configuration options"; for config in ${CONFIG_CHECK}; do die=1; error=0; negate=0; reworkmodulenames=0; if [[ ${config:0:1} == "~" ]]; then die=0; config=${config:1}; else if [[ ${config:0:1} == "@" ]]; then die=0; reworkmodulenames=1; config=${config:1}; fi; fi; if [[ ${config:0:1} == "!" ]]; then negate=1; config=${config:1}; fi; if [[ ${negate} == 1 ]]; then linux_chkconfig_present ${config} && error=2; else if [[ ${reworkmodulenames} == 1 ]]; then local temp_config="${config//*:}" i n; config="${config//:*}"; if linux_chkconfig_present ${config}; then for i in ${MODULE_NAMES}; do n="${i//${temp_config}}"; [[ -z ${n//\(*} ]] && MODULE_IGNORE="${MODULE_IGNORE} ${temp_config}"; done; error=2; fi; else linux_chkconfig_present ${config} || error=1; fi; fi; if [[ ${error} -gt 0 ]]; then local report_func="eerror" local_error; local_error="ERROR_${config}"; local_error="${!local_error}"; if [[ -z "${local_error}" ]]; then local_error="${config}_ERROR"; local_error="${!local_error}"; fi; if [[ ${die} == 0 && -z "${local_error}" ]]; then local_error="WARNING_${config}"; local_error="${!local_error}"; if [[ -n "${local_error}" ]]; then report_func="ewarn"; fi; fi; if [[ -z "${local_error}" ]]; then [[ ${error} == 1 ]] && local_error="is not set when it should be." || local_error="should not be set. But it is."; local_error="CONFIG_${config}:\t ${local_error}"; fi; if [[ ${die} == 0 ]]; then ${report_func} " ${local_error}"; soft_errors_count=$[soft_errors_count + 1]; else ${report_func} " ${local_error}"; hard_errors_count=$[hard_errors_count + 1]; fi; fi; done; if [[ ${hard_errors_count} -gt 0 ]]; then eend 1; eerror "Please check to make sure these options are set correctly."; eerror "Failure to do so may cause unexpected problems."; eerror "Once you have satisfied these options, please try merging"; eerror "this package again."; export LINUX_CONFIG_EXISTS_DONE="${old_LINUX_CONFIG_EXISTS_DONE}"; die "Incorrect kernel configuration options"; else if [[ ${soft_errors_count} -gt 0 ]]; then eend 1; ewarn "Please check to make sure these options are set correctly."; ewarn "Failure to do so may cause unexpected problems."; else eend 0; fi; fi; export LINUX_CONFIG_EXISTS_DONE="${old_LINUX_CONFIG_EXISTS_DONE}" } check_kernel_built () { if ! use kernel_linux; then die "${FUNCNAME}() called on non-Linux system, please fix the ebuild"; fi; [[ -n ${SKIP_KERNEL_CHECK} ]] && return; require_configured_kernel; local versionh_path; if kernel_is -ge 3 7; then versionh_path="include/generated/uapi/linux/version.h"; else versionh_path="include/linux/version.h"; fi; if [[ ! -f "${KV_OUT_DIR}/${versionh_path}" ]]; then eerror "These sources have not yet been prepared."; eerror "We cannot build against an unprepared tree."; eerror "To resolve this, please type the following:"; eerror; eerror "# cd ${KV_DIR}"; eerror "# make oldconfig"; eerror "# make modules_prepare"; eerror; eerror "Then please try merging this module again."; die "Kernel sources need compiling first"; fi } check_modules_supported () { if ! use kernel_linux; then die "${FUNCNAME}() called on non-Linux system, please fix the ebuild"; fi; require_configured_kernel; if ! linux_chkconfig_builtin "MODULES"; then eerror "These sources do not support loading external modules."; eerror "to be able to use this module please enable \"Loadable modules support\""; eerror "in your kernel, recompile and then try merging this module again."; die "No support for external modules in ${KV_FULL} config"; fi } check_zlibinflate () { if ! use kernel_linux; then die "${FUNCNAME}() called on non-Linux system, please fix the ebuild"; fi; require_configured_kernel; local INFLATE; local DEFLATE; einfo "Determining the usability of ZLIB_INFLATE support in your kernel"; ebegin "checking ZLIB_INFLATE"; linux_chkconfig_builtin CONFIG_ZLIB_INFLATE; eend $? || die; ebegin "checking ZLIB_DEFLATE"; linux_chkconfig_builtin CONFIG_ZLIB_DEFLATE; eend $? || die; local LINENO_START; local LINENO_END; local SYMBOLS; local x; LINENO_END="$(grep -n 'CONFIG_ZLIB_INFLATE y' ${KV_DIR}/lib/Config.in | cut -d : -f 1)"; LINENO_START="$(head -n $LINENO_END ${KV_DIR}/lib/Config.in | grep -n 'if \[' | tail -n 1 | cut -d : -f 1)"; (( LINENO_AMOUNT = ${LINENO_END} - ${LINENO_START} )); (( LINENO_END = ${LINENO_END} - 1 )); SYMBOLS="$(head -n $LINENO_END ${KV_DIR}/lib/Config.in | tail -n $LINENO_AMOUNT | sed -e 's/^.*\(CONFIG_[^\" ]*\).*/\1/g;')"; for x in ${SYMBOLS}; do if [[ "${!x}" = "y" ]]; then einfo "${x} ensures zlib is linked into your kernel - excellent"; return 0; fi; done; eerror; eerror "This kernel module requires ZLIB library support."; eerror "You have enabled zlib support in your kernel, but haven't enabled"; eerror "enabled any option that will ensure that zlib is linked into your"; eerror "kernel."; eerror; eerror "Please ensure that you enable at least one of these options:"; eerror; for x in ${SYMBOLS}; do eerror " * $x"; done; eerror; eerror "Please remember to recompile and install your kernel, and reboot"; eerror "into your new kernel before attempting to load this kernel module."; die "Kernel doesn't include zlib support" } clang-fullversion () { _clang_fullversion '$1.$2.$3' "$@" } clang-major-version () { _clang_fullversion '$1' "$@" } clang-micro-version () { _clang_fullversion '$3' "$@" } clang-minor-version () { _clang_fullversion '$2' "$@" } clang-version () { _clang_fullversion '$1.$2' "$@" } eapply () { local failed patch_cmd=patch; local -x LC_COLLATE=POSIX; type -P gpatch > /dev/null && patch_cmd=gpatch; function _eapply_patch () { local f=${1}; local prefix=${2}; ebegin "${prefix:-Applying }${f##*/}"; local all_opts=(-p1 -f -g0 --no-backup-if-mismatch "${patch_options[@]}"); if ${patch_cmd} "${all_opts[@]}" --dry-run -s -F0 < "${f}" &> /dev/null; then all_opts+=(-s -F0); fi; ${patch_cmd} "${all_opts[@]}" < "${f}"; failed=${?}; if ! eend "${failed}"; then __helpers_die "patch -p1 ${patch_options[*]} failed with ${f}"; fi }; local patch_options=() files=(); local i found_doublehyphen; for ((i = 1; i <= ${#@}; ++i )) do if [[ ${@:i:1} == -- ]]; then patch_options=("${@:1:i-1}"); files=("${@:i+1}"); found_doublehyphen=1; break; fi; done; if [[ -z ${found_doublehyphen} ]]; then for ((i = 1; i <= ${#@}; ++i )) do if [[ ${@:i:1} != -* ]]; then patch_options=("${@:1:i-1}"); files=("${@:i}"); break; fi; done; for i in "${files[@]}"; do if [[ ${i} == -* ]]; then die "eapply: all options must be passed before non-options"; fi; done; fi; if [[ ${#files[@]} -eq 0 ]]; then die "eapply: no files specified"; fi; local f; for f in "${files[@]}"; do if [[ -d ${f} ]]; then function _eapply_get_files () { local LC_ALL=POSIX; local prev_shopt=$(shopt -p nullglob); shopt -s nullglob; local f; for f in "${1}"/*; do if [[ ${f} == *.diff || ${f} == *.patch ]]; then files+=("${f}"); fi; done; ${prev_shopt} }; local files=(); _eapply_get_files "${f}"; [[ ${#files[@]} -eq 0 ]] && die "No *.{patch,diff} files in directory ${f}"; einfo "Applying patches from ${f} ..."; local f2; for f2 in "${files[@]}"; do _eapply_patch "${f2}" ' '; [[ ${failed} -ne 0 ]] && return "${failed}"; done; else _eapply_patch "${f}"; [[ ${failed} -ne 0 ]] && return "${failed}"; fi; done; return 0 } eapply_user () { [[ ${EBUILD_PHASE} == prepare ]] || die "eapply_user() called during invalid phase: ${EBUILD_PHASE}"; local tagfile=${T}/.portage_user_patches_applied; [[ -f ${tagfile} ]] && return; >> "${tagfile}"; local basedir=${PORTAGE_CONFIGROOT%/}/etc/portage/patches; local columns=${COLUMNS:-0}; [[ ${columns} == 0 ]] && columns=$(set -- $( ( stty size < /dev/tty ) 2> /dev/null || echo 24 80); echo $2); (( columns > 0 )) || (( columns = 80 )); local applied d f; local -A _eapply_user_patches; local prev_shopt=$(shopt -p nullglob); shopt -s nullglob; for d in "${basedir}"/${CATEGORY}/{${P}-${PR},${P},${PN}}{:${SLOT%/*},}; do for f in "${d}"/*; do if [[ ( ${f} == *.diff || ${f} == *.patch ) && -z ${_eapply_user_patches[${f##*/}]} ]]; then _eapply_user_patches[${f##*/}]=${f}; fi; done; done; if [[ ${#_eapply_user_patches[@]} -gt 0 ]]; then while read -r -d '' f; do f=${_eapply_user_patches[${f}]}; if [[ -s ${f} ]]; then if [[ -z ${applied} ]]; then einfo "${PORTAGE_COLOR_INFO}$(for ((column = 0; column < ${columns} - 3; column++)) do echo -n =; done)${PORTAGE_COLOR_NORMAL}"; einfo "Applying user patches from ${basedir} ..."; fi; eapply "${f}"; applied=1; fi; done < <(printf -- '%s\0' "${!_eapply_user_patches[@]}" | LC_ALL=C sort -z); fi; ${prev_shopt}; if [[ -n ${applied} ]]; then einfo "User patches applied."; einfo "${PORTAGE_COLOR_INFO}$(for ((column = 0; column < ${columns} - 3; column++)) do echo -n =; done)${PORTAGE_COLOR_NORMAL}"; fi } econf_build () { local CBUILD=${CBUILD:-${CHOST}}; function econf_env () { CHOST=${CBUILD} econf "$@" }; tc-env_build econf_env "$@" } edo () { einfo "$@"; "$@" || die -n "Failed to run command: $@" } edob () { ebegin "Running $@"; "$@"; eend $? || die -n "Failed to run command: $@" } einstalldocs () { ( if [[ $(declare -p DOCS 2> /dev/null) != *=* ]]; then local d; for d in README* ChangeLog AUTHORS NEWS TODO CHANGES THANKS BUGS FAQ CREDITS CHANGELOG; do [[ -f ${d} && -s ${d} ]] && docinto / && dodoc "${d}"; done; else if ___is_indexed_array_var DOCS; then [[ ${#DOCS[@]} -gt 0 ]] && docinto / && dodoc -r "${DOCS[@]}"; else [[ -n ${DOCS} ]] && docinto / && dodoc -r ${DOCS}; fi; fi ); ( if ___is_indexed_array_var HTML_DOCS; then [[ ${#HTML_DOCS[@]} -gt 0 ]] && docinto html && dodoc -r "${HTML_DOCS[@]}"; else [[ -n ${HTML_DOCS} ]] && docinto html && dodoc -r ${HTML_DOCS}; fi ) } filter-flags () { _filter-hardened "$@"; local v; for v in $(all-flag-vars); do _filter-var ${v} "$@"; done; return 0 } filter-ldflags () { _filter-var LDFLAGS "$@"; return 0 } filter-lfs-flags () { [[ $# -ne 0 ]] && die "filter-lfs-flags takes no arguments"; filter-flags -D_FILE_OFFSET_BITS=64 -D_LARGEFILE_SOURCE -D_LARGEFILE64_SOURCE -D_TIME_BITS=64 } filter-lto () { [[ $# -ne 0 ]] && die "filter-lto takes no arguments"; filter-flags '-flto*' -fwhole-program-vtables '-fsanitize=cfi*' } filter-mfpmath () { local orig_mfpmath new_math prune_math; orig_mfpmath=$(get-flag -mfpmath); new_math=$(get-flag mfpmath); new_math=${new_math/both/387,sse}; new_math=" ${new_math//[,+]/ } "; prune_math=""; for prune_math in "$@"; do new_math=${new_math/ ${prune_math} / }; done; new_math=$(echo ${new_math}); new_math=${new_math// /,}; if [[ -z ${new_math} ]]; then filter-flags ${orig_mfpmath}; else replace-flags ${orig_mfpmath} -mfpmath=${new_math}; fi; return 0 } gcc-fullversion () { _gcc_fullversion '$1.$2.$3' "$@" } gcc-major-version () { _gcc_fullversion '$1' "$@" } gcc-micro-version () { _gcc_fullversion '$3' "$@" } gcc-minor-version () { _gcc_fullversion '$2' "$@" } gcc-specs-directive () { local directive subdname subdirective; directive="$(_gcc-specs-directive_raw $1)"; while [[ ${directive} == *%\(*\)* ]]; do subdname=${directive/*%\(}; subdname=${subdname/\)*}; subdirective="$(_gcc-specs-directive_raw ${subdname})"; directive="${directive//\%(${subdname})/${subdirective}}"; done; echo "${directive}"; return 0 } gcc-specs-nostrict () { local directive; directive=$(gcc-specs-directive cc1); [[ "${directive/\{!fstrict-overflow:}" != "${directive}" ]] } gcc-specs-now () { local directive; directive=$(gcc-specs-directive link_command); [[ "${directive/\{!nonow:}" != "${directive}" ]] } gcc-specs-pie () { local directive; directive=$(gcc-specs-directive cc1); [[ "${directive/\{!nopie:}" != "${directive}" ]] } gcc-specs-relro () { local directive; directive=$(gcc-specs-directive link_command); [[ "${directive/\{!norelro:}" != "${directive}" ]] } gcc-specs-ssp () { local directive; directive=$(gcc-specs-directive cc1); [[ "${directive/\{!fno-stack-protector:}" != "${directive}" ]] } gcc-specs-ssp-to-all () { local directive; directive=$(gcc-specs-directive cc1); [[ "${directive/\{!fno-stack-protector-all:}" != "${directive}" ]] } gcc-specs-stack-check () { local directive; directive=$(gcc-specs-directive cc1); [[ "${directive/\{!fno-stack-check:}" != "${directive}" ]] } gcc-version () { _gcc_fullversion '$1.$2' "$@" } gen_usr_ldscript () { ewarn "${FUNCNAME}: Please migrate to usr-ldscript.eclass"; local lib libdir=$(get_libdir) output_format="" auto=false suffix=$(get_libname); [[ -z ${ED+set} ]] && local ED=${D%/}${EPREFIX}/; tc-is-static-only && return; if [[ $(type -t multilib_is_native_abi) == "function" ]]; then multilib_is_native_abi || return 0; fi; case ${CTARGET:-${CHOST}} in *-darwin*) ;; *-android*) return 0 ;; *linux*) use prefix && return 0 ;; *) return 0 ;; esac; dodir /usr/${libdir}; if [[ $1 == "-a" ]]; then auto=true; shift; dodir /${libdir}; fi; local flags=(${CFLAGS} ${LDFLAGS} -Wl,--verbose); if $(tc-getLD) --version | grep -q 'GNU gold'; then local d="${T}/bfd-linker"; mkdir -p "${d}"; ln -sf $(type -P ${CHOST}-ld.bfd) "${d}"/ld; flags+=(-B"${d}"); fi; output_format=$($(tc-getCC) "${flags[@]}" 2>&1 | sed -n 's/^OUTPUT_FORMAT("\([^"]*\)",.*/\1/p'); [[ -n ${output_format} ]] && output_format="OUTPUT_FORMAT ( ${output_format} )"; for lib in "$@"; do local tlib; if ${auto}; then lib="lib${lib}${suffix}"; else [[ -r ${ED}/${libdir}/${lib} ]] || continue; fi; case ${CTARGET:-${CHOST}} in *-darwin*) if ${auto}; then tlib=$(scanmacho -qF'%S#F' "${ED}"/usr/${libdir}/${lib}); else tlib=$(scanmacho -qF'%S#F' "${ED}"/${libdir}/${lib}); fi; [[ -z ${tlib} ]] && die "unable to read install_name from ${lib}"; tlib=${tlib##*/}; if ${auto}; then mv "${ED}"/usr/${libdir}/${lib%${suffix}}.*${suffix#.} "${ED}"/${libdir}/ || die; if [[ ${tlib} != ${lib%${suffix}}.*${suffix#.} ]]; then mv "${ED}"/usr/${libdir}/${tlib%${suffix}}.*${suffix#.} "${ED}"/${libdir}/ || die; fi; rm -f "${ED}"/${libdir}/${lib}; fi; if [[ ! -w "${ED}/${libdir}/${tlib}" ]]; then chmod u+w "${ED}${libdir}/${tlib}"; local nowrite=yes; fi; install_name_tool -id "${EPREFIX}"/${libdir}/${tlib} "${ED}"/${libdir}/${tlib} || die "install_name_tool failed"; [[ -n ${nowrite} ]] && chmod u-w "${ED}${libdir}/${tlib}"; pushd "${ED}/usr/${libdir}" > /dev/null; ln -snf "../../${libdir}/${tlib}" "${lib}"; popd > /dev/null ;; *) if ${auto}; then tlib=$(scanelf -qF'%S#F' "${ED}"/usr/${libdir}/${lib}); [[ -z ${tlib} ]] && die "unable to read SONAME from ${lib}"; mv "${ED}"/usr/${libdir}/${lib}* "${ED}"/${libdir}/ || die; if [[ ${tlib} != ${lib}* ]]; then mv "${ED}"/usr/${libdir}/${tlib}* "${ED}"/${libdir}/ || die; fi; rm -f "${ED}"/${libdir}/${lib}; else tlib=${lib}; fi; cat > "${ED}/usr/${libdir}/${lib}" <<-END_LDSCRIPT /* GNU ld script Since Gentoo has critical dynamic libraries in /lib, and the static versions in /usr/lib, we need to have a "fake" dynamic lib in /usr/lib, otherwise we run into linking problems. This "fake" dynamic lib is a linker script that redirects the linker to the real lib. And yes, this works in the cross- compiling scenario as the sysroot-ed linker will prepend the real path. See bug https://bugs.gentoo.org/4411 for more info. */ ${output_format} GROUP ( ${EPREFIX}/${libdir}/${tlib} ) END_LDSCRIPT ;; esac fperms a+x "/usr/${libdir}/${lib}" || die "could not change perms on ${lib}"; done } get-flag () { [[ $# -ne 1 ]] && die "usage: "; local f var findflag="$1"; for var in $(all-flag-vars); do for f in ${!var}; do if [ "${f/${findflag}}" != "${f}" ]; then printf "%s\n" "${f/-${findflag}=}"; return 0; fi; done; done; return 1 } get_abi_CFLAGS () { get_abi_var CFLAGS "$@" } get_abi_CHOST () { get_abi_var CHOST "$@" } get_abi_CTARGET () { get_abi_var CTARGET "$@" } get_abi_FAKE_TARGETS () { get_abi_var FAKE_TARGETS "$@" } get_abi_LDFLAGS () { get_abi_var LDFLAGS "$@" } get_abi_LIBDIR () { get_abi_var LIBDIR "$@" } get_abi_var () { local flag=$1; local abi=${2:-${ABI:-${DEFAULT_ABI:-default}}}; local var="${flag}_${abi}"; echo ${!var} } get_all_abis () { local x order="" mvar dvar; mvar="MULTILIB_ABIS"; dvar="DEFAULT_ABI"; if [[ -n $1 ]]; then mvar="$1_${mvar}"; dvar="$1_${dvar}"; fi; if [[ -z ${!mvar} ]]; then echo "default"; return 0; fi; for x in ${!mvar}; do if [[ ${x} != ${!dvar} ]]; then order="${order:+${order} }${x}"; fi; done; order="${order:+${order} }${!dvar}"; echo ${order}; return 0 } get_all_libdirs () { local libdirs abi; for abi in ${MULTILIB_ABIS}; do libdirs+=" $(get_abi_LIBDIR ${abi})"; done; [[ " ${libdirs} " != *" lib "* ]] && libdirs+=" lib"; echo "${libdirs}" } get_exeext () { case ${CHOST} in mingw* | *-mingw*) echo ".exe" ;; esac } get_install_abis () { local x order=""; if [[ -z ${MULTILIB_ABIS} ]]; then echo "default"; return 0; fi; if [[ ${EMULTILIB_PKG} == "true" ]]; then for x in ${MULTILIB_ABIS}; do if [[ ${x} != "${DEFAULT_ABI}" ]]; then has ${x} ${ABI_DENY} || order="${order} ${x}"; fi; done; has ${DEFAULT_ABI} ${ABI_DENY} || order="${order} ${DEFAULT_ABI}"; if [[ -n ${ABI_ALLOW} ]]; then local ordera=""; for x in ${order}; do if has ${x} ${ABI_ALLOW}; then ordera="${ordera} ${x}"; fi; done; order=${ordera}; fi; else order=${DEFAULT_ABI}; fi; if [[ -z ${order} ]]; then die "The ABI list is empty. Are you using a proper multilib profile? Perhaps your USE flags or MULTILIB_ABIS are too restrictive for this package."; fi; echo ${order}; return 0 } get_libdir () { local libdir_var="LIBDIR_${ABI}"; local libdir="lib"; [[ -n ${ABI} && -n ${!libdir_var} ]] && libdir=${!libdir_var}; echo "${libdir}" } get_libname () { local libname; local ver=$1; case ${CHOST} in mingw* | *-mingw*) libname="dll" ;; *-darwin*) libname="dylib" ;; *) libname="so" ;; esac; if [[ -z $* ]]; then echo ".${libname}"; else for ver in "$@"; do case ${CHOST} in *-darwin*) echo ".${ver}.${libname}" ;; *) echo ".${libname}.${ver}" ;; esac; done; fi } get_makefile_extract_function () { [[ -n ${SKIP_KERNEL_CHECK} ]] && return; local a='' b='' mkfunc='getfilevar'; a="$(getfilevar VERSION ${KERNEL_MAKEFILE})"; b="$(getfilevar_noexec VERSION ${KERNEL_MAKEFILE})"; [[ "${a}" != "${b}" ]] && mkfunc='getfilevar_noexec'; echo "${mkfunc}" } get_modname () { local modname; local ver=$1; case ${CHOST} in *-darwin*) modname="bundle" ;; *) modname="so" ;; esac; echo ".${modname}" } get_nproc () { local nproc; if type -P nproc &> /dev/null; then nproc=$(nproc); fi; if [[ -z ${nproc} ]] && type -P sysctl &> /dev/null; then nproc=$(sysctl -n hw.ncpu 2> /dev/null); fi; if [[ -z ${nproc} ]] && type -P python &> /dev/null; then nproc=$(python -c 'import multiprocessing; print(multiprocessing.cpu_count());' 2> /dev/null); fi; if [[ -n ${nproc} ]]; then echo "${nproc}"; else echo "${1:-1}"; fi } get_running_version () { if ! use kernel_linux; then die "${FUNCNAME}() called on non-Linux system, please fix the ebuild"; fi; local kv=$(uname -r); if [[ -f ${ROOT%/}/lib/modules/${kv}/source/Makefile ]]; then KERNEL_DIR=$(readlink -f "${ROOT%/}/lib/modules/${kv}/source"); if [[ -f ${ROOT%/}/lib/modules/${kv}/build/Makefile ]]; then KBUILD_OUTPUT=$(readlink -f "${ROOT%/}/lib/modules/${kv}/build"); fi; get_version && return 0; fi; KV_FULL=${kv}; local kv_full=${KV_FULL//[-+_]*}; KV_MAJOR=$(ver_cut 1 ${kv_full}); KV_MINOR=$(ver_cut 2 ${kv_full}); KV_PATCH=$(ver_cut 3 ${kv_full}); KV_EXTRA="${KV_FULL#${KV_MAJOR}.${KV_MINOR}${KV_PATCH:+.${KV_PATCH}}}"; : "${KV_PATCH:=0}"; return 0 } get_version () { if ! use kernel_linux; then die "${FUNCNAME}() called on non-Linux system, please fix the ebuild"; fi; local tmplocal; [[ -n ${SKIP_KERNEL_CHECK} ]] && return; [[ -n "${KV_FULL}" ]] && return 0; unset KV_DIR; [[ -z "${get_version_warning_done}" ]] && qeinfo "Determining the location of the kernel source code"; [[ -d "${KERNEL_DIR}" ]] && KV_DIR="${KERNEL_DIR}"; if [[ -z "${KV_DIR}" ]]; then if [[ -z "${get_version_warning_done}" ]]; then get_version_warning_done=1; qewarn "Unable to find kernel sources at ${KERNEL_DIR}"; if [[ "${KERNEL_DIR}" == "/usr/src/linux" ]]; then qeinfo "Please make sure that ${KERNEL_DIR} points at your running kernel, "; qeinfo "(or the kernel you wish to build against)."; qeinfo "Alternatively, set the KERNEL_DIR environment variable to the kernel sources location"; else qeinfo "Please ensure that the KERNEL_DIR environment variable points at full Linux sources of the kernel you wish to compile against."; fi; fi; return 1; fi; if [[ -z "${KBUILD_OUTPUT}" && -L "${KERNEL_DIR}/source" ]]; then KBUILD_OUTPUT=${KERNEL_DIR}; KERNEL_DIR=$(readlink -f "${KERNEL_DIR}/source"); KV_DIR=${KERNEL_DIR}; fi; if [[ -z "${get_version_warning_done}" ]]; then qeinfo "Found kernel source directory:"; qeinfo " ${KV_DIR}"; fi; kernel_get_makefile; if [[ ! -s ${KERNEL_MAKEFILE} ]]; then if [[ -z "${get_version_warning_done}" ]]; then get_version_warning_done=1; qeerror "Could not find a Makefile in the kernel source directory."; qeerror "Please ensure that ${KERNEL_DIR} points to a complete set of Linux sources"; fi; return 1; fi; local OUTPUT_DIR=${KBUILD_OUTPUT}; if [[ -z ${OUTPUT_DIR} ]]; then local mkfunc=$(get_makefile_extract_function "${KERNEL_MAKEFILE}"); OUTPUT_DIR=$(${mkfunc} KBUILD_OUTPUT "${KERNEL_MAKEFILE}"); fi; KV_MAJOR=$(getfilevar VERSION "${KERNEL_MAKEFILE}"); KV_MINOR=$(getfilevar PATCHLEVEL "${KERNEL_MAKEFILE}"); KV_PATCH=$(getfilevar SUBLEVEL "${KERNEL_MAKEFILE}"); KV_EXTRA=$(getfilevar EXTRAVERSION "${KERNEL_MAKEFILE}"); if [[ -z "${KV_MAJOR}" || -z "${KV_MINOR}" || -z "${KV_PATCH}" ]]; then if [[ -z "${get_version_warning_done}" ]]; then get_version_warning_done=1; qeerror "Could not detect kernel version."; qeerror "Please ensure that ${KERNEL_DIR} points to a complete set of Linux sources."; fi; return 1; fi; [[ -d "${OUTPUT_DIR}" ]] && KV_OUT_DIR="${OUTPUT_DIR}"; if [[ -n "${KV_OUT_DIR}" ]]; then qeinfo "Found kernel object directory:"; qeinfo " ${KV_OUT_DIR}"; fi; KV_OUT_DIR="${KV_OUT_DIR:-${KV_DIR}}"; if [[ -s "${KV_OUT_DIR}"/include/config/kernel.release ]]; then KV_LOCAL=$(< "${KV_OUT_DIR}"/include/config/kernel.release); else if [[ -s "${KV_OUT_DIR}"/.kernelrelease ]]; then KV_LOCAL=$(< "${KV_OUT_DIR}"/.kernelrelease); else KV_LOCAL=; fi; fi; tmplocal=${KV_LOCAL#${KV_MAJOR}.${KV_MINOR}.${KV_PATCH}${KV_EXTRA}}; if [[ "${KV_LOCAL}" = "${tmplocal}" ]]; then KV_LOCAL=; else KV_LOCAL=${tmplocal}; fi; if [[ -z ${OUTPUT_DIR} ]]; then for OUTPUT_DIR in "${SYSROOT}" "${ROOT%/}" ""; do OUTPUT_DIR+="/lib/modules/${KV_MAJOR}.${KV_MINOR}.${KV_PATCH}${KV_EXTRA}${KV_LOCAL}/build"; if [[ -e ${OUTPUT_DIR} ]]; then break; fi; done; fi; KV_FULL="${KV_MAJOR}.${KV_MINOR}.${KV_PATCH}${KV_EXTRA}${KV_LOCAL}"; qeinfo "Found sources for kernel version:"; qeinfo " ${KV_FULL}"; return 0 } getfilevar () { local ERROR basefname basedname myARCH="${ARCH}"; ERROR=0; [[ -z "${1}" ]] && ERROR=1; [[ ! -f "${2}" ]] && ERROR=1; if [[ "${ERROR}" = 1 ]]; then echo -e "\n"; eerror "getfilevar requires 2 variables, with the second a valid file."; eerror " getfilevar "; else basefname="$(basename ${2})"; basedname="$(dirname ${2})"; unset ARCH; echo -e "e:\\n\\t@echo \$(${1})\\ninclude ${basefname}" | nonfatal emake -C "${basedname}" --no-print-directory M="${T}" dot-config=0 need-config= need-compiler= ${BUILD_FIXES} -s -f - 2> /dev/null; ARCH=${myARCH}; fi } getfilevar_noexec () { local ERROR basefname basedname mycat myARCH="${ARCH}"; ERROR=0; mycat='cat'; [[ -z "${1}" ]] && ERROR=1; [[ ! -f "${2}" ]] && ERROR=1; [[ "${2%.gz}" != "${2}" ]] && mycat='zcat'; if [[ "${ERROR}" = 1 ]]; then echo -e "\n"; eerror "getfilevar_noexec requires 2 variables, with the second a valid file."; eerror " getfilevar_noexec "; else ${mycat} "${2}" | sed -n -e "/^[[:space:]]*${1}[[:space:]]*:\\?=[[:space:]]*\(.*\)\$/{ s,^[^=]*[[:space:]]*=[[:space:]]*,,g ; s,[[:space:]]*\$,,g ; p }"; fi } has_multilib_profile () { [ -n "${MULTILIB_ABIS}" -a "${MULTILIB_ABIS}" != "${MULTILIB_ABIS/ /}" ] } in_iuse () { local use=${1}; if [[ -z "${use}" ]]; then echo "!!! in_iuse() called without a parameter." 1>&2; echo "!!! in_iuse " 1>&2; die "in_iuse() called without a parameter"; fi; local liuse=(${IUSE_EFFECTIVE}); has "${use}" "${liuse[@]#[+-]}" } is-flag () { is-flagq "$@" && echo true } is-flagq () { [[ -n $2 ]] && die "Usage: is-flag "; local var; for var in $(all-flag-vars); do _is_flagq ${var} "$1" && return 0; done; return 1 } is-ldflag () { is-ldflagq "$@" && echo true } is-ldflagq () { [[ -n $2 ]] && die "Usage: is-ldflag "; _is_flagq LDFLAGS $1 } is_final_abi () { has_multilib_profile || return 0; set -- $(get_install_abis); local LAST_ABI=$#; [[ ${!LAST_ABI} == ${ABI} ]] } kernel_get_makefile () { [[ -s ${KV_DIR}/GNUMakefile ]] && KERNEL_MAKEFILE="${KV_DIR}/GNUMakefile" && return; [[ -s ${KV_DIR}/makefile ]] && KERNEL_MAKEFILE="${KV_DIR}/makefile" && return; [[ -s ${KV_DIR}/Makefile ]] && KERNEL_MAKEFILE="${KV_DIR}/Makefile" && return } kernel_is () { if ! use kernel_linux; then die "${FUNCNAME}() called on non-Linux system, please fix the ebuild"; fi; linux-info_get_any_version; local operator; case ${1#-} in lt) operator="-lt"; shift ;; gt) operator="-gt"; shift ;; le) operator="-le"; shift ;; ge) operator="-ge"; shift ;; eq) operator="-eq"; shift ;; *) operator="-eq" ;; esac; [[ $# -gt 3 ]] && die "Error in ${ECLASS}_${FUNCNAME}(): too many parameters"; ver_test "${KV_MAJOR:-0}.${KV_MINOR:-0}.${KV_PATCH:-0}" "${operator}" "${1:-${KV_MAJOR:-0}}.${2:-${KV_MINOR:-0}}.${3:-${KV_PATCH:-0}}" } linux-info_get_any_version () { if ! use kernel_linux; then die "${FUNCNAME}() called on non-Linux system, please fix the ebuild"; fi; if ! get_version; then ewarn "Unable to calculate Linux Kernel version for build, attempting to use running version"; if ! get_running_version; then die "Unable to determine any Linux Kernel version, please report a bug"; fi; fi } linux-info_pkg_setup () { use kernel_linux || return; linux-info_get_any_version; [[ -n "${CONFIG_CHECK}" && -z ${CHECKCONFIG_DONOTHING} ]] && check_extra_config } linux-mod-r1_pkg_postinst () { debug-print-function ${FUNCNAME[0]} "${@}"; _modules_check_function ${#} 0 0 || return 0; _modules_update_depmod; [[ -v _MODULES_GLOBAL[ran:post_process] ]] || eqawarn "QA Notice: neither linux-mod-r1_src_install nor modules_post_process were used" } linux-mod-r1_pkg_setup () { debug-print-function ${FUNCNAME[0]} "${@}"; [[ ${MERGE_TYPE} != binary ]] || return 0; _MODULES_GLOBAL[ran:pkg_setup]=1; _modules_check_function ${#} 0 0 || return 0; _modules_check_migration; _modules_prepare_kernel; _modules_prepare_sign; _modules_prepare_toolchain; _modules_set_makeargs; _modules_sanity_gccplugins } linux-mod-r1_src_compile () { debug-print-function ${FUNCNAME[0]} "${@}"; _modules_check_function ${#} 0 0 || return 0; [[ ${modlist@a} == *a* && ${#modlist[@]} -gt 0 ]] || die "${FUNCNAME[0]} was called without a 'modlist' array"; _modules_sanity_kernelbuilt; local -a emakeargs=("${MODULES_MAKEARGS[@]}"); [[ ${modargs@a} == *a* ]] && emakeargs+=("${modargs[@]}"); local -A built=(); local build mod name target; for mod in "${modlist[@]}"; do name=${mod%%=*}; [[ -n ${name} && ${name} != *:* ]] || die "invalid mod entry '${mod}'"; mod=${mod#"${name}"}; IFS=: read -ra mod <<< "${mod#=}"; [[ ${#mod[@]} -le 4 ]] || die "too many ':' in ${name}'s modlist"; [[ ${mod[1]:=${PWD}} != /* ]] && mod[1]=${PWD}/${mod[1]}; [[ ${mod[2]:=${mod[1]}} != /* ]] && mod[2]=${PWD}/${mod[2]}; _MODULES_INSTALL[${mod[2]}/${name}.ko]=${mod[0]:-extra}; pushd "${mod[1]}" > /dev/null || die; if [[ -z ${mod[3]} ]]; then for target in module{s,} "${name}".ko default all; do nonfatal emake "${emakeargs[@]}" -q "${target}" &> /dev/null; if [[ ${?} -eq 1 ]]; then mod[3]=${target}; break; fi; done; fi; build=; for target in ${mod[3]:-&}; do if ! has "${target}" ${built[${mod[1]}]}; then build=1; built[${mod[1]}]+=" ${target} "; fi; done; if [[ -n ${build} ]]; then einfo "Building ${name} module in ${mod[1]} ..."; emake "${emakeargs[@]}" ${mod[3]}; else einfo "Building ${name} module in ${mod[1]} ... already done."; fi; popd > /dev/null || die; done } linux-mod-r1_src_install () { debug-print-function ${FUNCNAME[0]} "${@}"; _modules_check_function ${#} 0 0 || return 0; (( ${#_MODULES_INSTALL[@]} )) || die "${FUNCNAME[0]} was called without running linux-mod-r1_src_compile"; ( for mod in "${!_MODULES_INSTALL[@]}"; do linux_moduleinto "${_MODULES_INSTALL[${mod}]}"; linux_domodule "${mod}"; done ); modules_post_process; einstalldocs } linux_chkconfig_builtin () { [[ -n ${SKIP_KERNEL_CHECK} ]] && return; linux_config_qa_check linux_chkconfig_builtin; [[ $(getfilevar_noexec "CONFIG_$1" "$(linux_config_path)") == y ]] } linux_chkconfig_module () { [[ -n ${SKIP_KERNEL_CHECK} ]] && return; linux_config_qa_check linux_chkconfig_module; [[ $(getfilevar_noexec "CONFIG_$1" "$(linux_config_path)") == m ]] } linux_chkconfig_present () { [[ -n ${SKIP_KERNEL_CHECK} ]] && return; linux_config_qa_check linux_chkconfig_present; [[ $(getfilevar_noexec "CONFIG_$1" "$(linux_config_path)") == [my] ]] } linux_chkconfig_string () { [[ -n ${SKIP_KERNEL_CHECK} ]] && return; linux_config_qa_check linux_chkconfig_string; getfilevar_noexec "CONFIG_$1" "$(linux_config_path)" } linux_config_bin_exists () { export _LINUX_CONFIG_EXISTS_DONE=1; use kernel_linux && [[ -s /proc/config.gz ]] } linux_config_exists () { linux_config_src_exists || linux_config_bin_exists } linux_config_path () { if linux_config_src_exists; then echo "${KV_OUT_DIR}/.config"; else if linux_config_bin_exists; then echo "/proc/config.gz"; else return 1; fi; fi } linux_config_qa_check () { local f="$1"; if [[ -z "${_LINUX_CONFIG_EXISTS_DONE}" ]]; then ewarn "QA: You called $f before any linux_config_exists!"; ewarn "QA: The return value of $f will NOT guaranteed later!"; fi; if ! use kernel_linux; then die "$f called on non-Linux system, please fix the ebuild"; fi } linux_config_src_exists () { export _LINUX_CONFIG_EXISTS_DONE=1; use kernel_linux && [[ -n ${KV_OUT_DIR} && -s ${KV_OUT_DIR}/.config ]] } linux_domodule () { debug-print-function ${FUNCNAME[0]} "${@}"; _modules_check_function ${#} 1 '' "..." || return 0; ( insinto "/lib/modules/${KV_FULL}/${_MODULES_GLOBAL[moduleinto]:-extra}"; doins "${@}" ) } linux_moduleinto () { debug-print-function ${FUNCNAME[0]} "${@}"; _modules_check_function ${#} 1 1 "" || return 0; _MODULES_GLOBAL[moduleinto]=${1} } makeopts_jobs () { [[ $# -eq 0 ]] && set -- "${MAKEOPTS}"; local jobs=$(echo " $* " | sed -r -n -e 's:.*[[:space:]](-[a-z]*j|--jobs[=[:space:]])[[:space:]]*([0-9]+).*:\2:p' -e "s:.*[[:space:]](-[a-z]*j|--jobs)[[:space:]].*:${2:-$(( $(get_nproc) + 1 ))}:p"); echo ${jobs:-1} } makeopts_loadavg () { [[ $# -eq 0 ]] && set -- "${MAKEOPTS}"; local lavg=$(echo " $* " | sed -r -n -e 's:.*[[:space:]](-[a-z]*l|--(load-average|max-load)[=[:space:]])[[:space:]]*([0-9]+(\.[0-9]+)?)[[:space:]].*:\3:p' -e "s:.*[[:space:]](-[a-z]*l|--(load-average|max-load))[[:space:]].*:${2:-999}:p"); echo ${lavg:-${2:-999}} } modules_post_process () { debug-print-function ${FUNCNAME[0]} "${@}"; _modules_check_function ${#} 0 1 '[]' || return 0; [[ ${EBUILD_PHASE} == install ]] || die "${FUNCNAME[0]} can only be called in the src_install phase"; local path=${ED}${1-/lib/modules/${KV_FULL}}; local -a mods; [[ -d ${path} ]] && mapfile -td '' mods < <(find "${path}" -type f -name '*.ko' -print0 || die); (( ${#mods[@]} )) || die "${FUNCNAME[0]} was called with no installed modules under ${path}"; _modules_process_strip "${mods[@]}"; _modules_process_sign "${mods[@]}"; _modules_sanity_modversion "${mods[@]}"; _modules_process_compress "${mods[@]}"; _MODULES_GLOBAL[ran:post_process]=1 } multilib_env () { local CTARGET=${1:-${CTARGET}}; local cpu=${CTARGET%%*-}; if [[ ${CTARGET} = *-musl* ]]; then : "${MULTILIB_ABIS=default}"; : "${DEFAULT_ABI=default}"; export MULTILIB_ABIS DEFAULT_ABI; return; fi; case ${cpu} in aarch64*) export CFLAGS_arm=${CFLAGS_arm-}; case ${cpu} in aarch64*be) export CHOST_arm="armv8b-${CTARGET#*-}" ;; *) export CHOST_arm="armv8l-${CTARGET#*-}" ;; esac; CHOST_arm=${CHOST_arm/%-gnu/-gnueabi}; export CTARGET_arm=${CHOST_arm}; export LIBDIR_arm="lib"; export CFLAGS_arm64=${CFLAGS_arm64-}; export CHOST_arm64=${CTARGET}; export CTARGET_arm64=${CHOST_arm64}; export LIBDIR_arm64="lib64"; : "${MULTILIB_ABIS=arm64}"; : "${DEFAULT_ABI=arm64}" ;; x86_64*) export CFLAGS_x86=${CFLAGS_x86--m32}; export CHOST_x86=${CTARGET/x86_64/i686}; CHOST_x86=${CHOST_x86/%-gnux32/-gnu}; export CTARGET_x86=${CHOST_x86}; if [[ ${SYMLINK_LIB} == "yes" ]]; then export LIBDIR_x86="lib32"; else export LIBDIR_x86="lib"; fi; export CFLAGS_amd64=${CFLAGS_amd64--m64}; export CHOST_amd64=${CTARGET/%-gnux32/-gnu}; export CTARGET_amd64=${CHOST_amd64}; export LIBDIR_amd64="lib64"; export CFLAGS_x32=${CFLAGS_x32--mx32}; export CHOST_x32=${CTARGET/%-gnu/-gnux32}; export CTARGET_x32=${CHOST_x32}; export LIBDIR_x32="libx32"; case ${CTARGET} in *-gnux32) : "${MULTILIB_ABIS=x32 amd64 x86}"; : "${DEFAULT_ABI=x32}" ;; *) : "${MULTILIB_ABIS=amd64 x86}"; : "${DEFAULT_ABI=amd64}" ;; esac ;; loongarch64*) export CFLAGS_lp64d=${CFLAGS_lp64d--mabi=lp64d}; export CHOST_lp64d=${CTARGET}; export CTARGET_lp64d=${CTARGET}; export LIBDIR_lp64d=${LIBDIR_lp64d-lib64}; : "${MULTILIB_ABIS=lp64d}"; : "${DEFAULT_ABI=lp64d}" ;; mips64* | mipsisa64*) export CFLAGS_o32=${CFLAGS_o32--mabi=32}; export CHOST_o32=${CTARGET/mips64/mips}; export CHOST_o32=${CHOST_o32/mipsisa64/mipsisa32}; export CTARGET_o32=${CHOST_o32}; export LIBDIR_o32="lib"; export CFLAGS_n32=${CFLAGS_n32--mabi=n32}; export CHOST_n32=${CTARGET}; export CTARGET_n32=${CHOST_n32}; export LIBDIR_n32="lib32"; export CFLAGS_n64=${CFLAGS_n64--mabi=64}; export CHOST_n64=${CTARGET}; export CTARGET_n64=${CHOST_n64}; export LIBDIR_n64="lib64"; : "${MULTILIB_ABIS=n64 n32 o32}"; : "${DEFAULT_ABI=n32}" ;; powerpc64*) export CFLAGS_ppc=${CFLAGS_ppc--m32}; export CHOST_ppc=${CTARGET/powerpc64/powerpc}; export CTARGET_ppc=${CHOST_ppc}; export LIBDIR_ppc="lib"; export CFLAGS_ppc64=${CFLAGS_ppc64--m64}; export CHOST_ppc64=${CTARGET}; export CTARGET_ppc64=${CHOST_ppc64}; export LIBDIR_ppc64="lib64"; : "${MULTILIB_ABIS=ppc64 ppc}"; : "${DEFAULT_ABI=ppc64}" ;; riscv64*) : "${MULTILIB_ABIS=lp64d lp64 ilp32d ilp32}"; : "${DEFAULT_ABI=lp64d}"; local _libdir_riscvdefaultabi_variable="LIBDIR_${DEFAULT_ABI}"; local _libdir_riscvdefaultabi=${!_libdir_riscvdefaultabi_variable}; export ${_libdir_riscvdefaultabi_variable}=${_libdir_riscvdefaultabi:-lib64}; export CFLAGS_lp64d=${CFLAGS_lp64d--mabi=lp64d -march=rv64gc}; export CHOST_lp64d=${CTARGET}; export CTARGET_lp64d=${CTARGET}; export LIBDIR_lp64d=${LIBDIR_lp64d-lib64/lp64d}; export CFLAGS_lp64=${CFLAGS_lp64--mabi=lp64 -march=rv64imac}; export CHOST_lp64=${CTARGET}; export CTARGET_lp64=${CTARGET}; export LIBDIR_lp64=${LIBDIR_lp64-lib64/lp64}; export CFLAGS_ilp32d=${CFLAGS_ilp32d--mabi=ilp32d -march=rv32imafdc}; export CHOST_ilp32d=${CTARGET/riscv64/riscv32}; export CTARGET_ilp32d=${CTARGET/riscv64/riscv32}; export LIBDIR_ilp32d=${LIBDIR_ilp32d-lib32/ilp32d}; export CFLAGS_ilp32=${CFLAGS_ilp32--mabi=ilp32 -march=rv32imac}; export CHOST_ilp32=${CTARGET/riscv64/riscv32}; export CTARGET_ilp32=${CTARGET/riscv64/riscv32}; export LIBDIR_ilp32=${LIBDIR_ilp32-lib32/ilp32} ;; riscv32*) : "${MULTILIB_ABIS=ilp32d ilp32}"; : "${DEFAULT_ABI=ilp32d}"; local _libdir_riscvdefaultabi_variable="LIBDIR_${DEFAULT_ABI}"; local _libdir_riscvdefaultabi=${!_libdir_riscvdefaultabi_variable}; export ${_libdir_riscvdefaultabi_variable}=${_libdir_riscvdefaultabi:-lib}; export CFLAGS_ilp32d=${CFLAGS_ilp32d--mabi=ilp32d -march=rv32imafdc}; export CHOST_ilp32d=${CTARGET}; export CTARGET_ilp32d=${CTARGET}; export LIBDIR_ilp32d=${LIBDIR_ilp32d-lib32/ilp32d}; export CFLAGS_ilp32=${CFLAGS_ilp32--mabi=ilp32 -march=rv32imac}; export CHOST_ilp32=${CTARGET}; export CTARGET_ilp32=${CTARGET}; export LIBDIR_ilp32=${LIBDIR_ilp32-lib32/ilp32} ;; s390x*) export CFLAGS_s390=${CFLAGS_s390--m31}; export CHOST_s390=${CTARGET/s390x/s390}; export CTARGET_s390=${CHOST_s390}; export LIBDIR_s390="lib"; export CFLAGS_s390x=${CFLAGS_s390x--m64}; export CHOST_s390x=${CTARGET}; export CTARGET_s390x=${CHOST_s390x}; export LIBDIR_s390x="lib64"; : "${MULTILIB_ABIS=s390x s390}"; : "${DEFAULT_ABI=s390x}" ;; sparc64*) export CFLAGS_sparc32=${CFLAGS_sparc32--m32}; export CHOST_sparc32=${CTARGET/sparc64/sparc}; export CTARGET_sparc32=${CHOST_sparc32}; export LIBDIR_sparc32="lib"; export CFLAGS_sparc64=${CFLAGS_sparc64--m64}; export CHOST_sparc64=${CTARGET}; export CTARGET_sparc64=${CHOST_sparc64}; export LIBDIR_sparc64="lib64"; : "${MULTILIB_ABIS=sparc64 sparc32}"; : "${DEFAULT_ABI=sparc64}" ;; *) : "${MULTILIB_ABIS=default}"; : "${DEFAULT_ABI=default}" ;; esac; export MULTILIB_ABIS DEFAULT_ABI } multilib_toolchain_setup () { local v vv; export ABI=$1; local save_restore_variables=(CBUILD CHOST AR CC CXX F77 FC LD NM OBJCOPY OBJDUMP PKG_CONFIG RANLIB READELF STRINGS STRIP PKG_CONFIG_LIBDIR PKG_CONFIG_PATH PKG_CONFIG_SYSTEM_INCLUDE_PATH PKG_CONFIG_SYSTEM_LIBRARY_PATH); if [[ ${_DEFAULT_ABI_SAVED} == "true" ]]; then for v in "${save_restore_variables[@]}"; do vv="_abi_saved_${v}"; [[ ${!vv+set} == "set" ]] && export ${v}="${!vv}" || unset ${v}; unset ${vv}; done; unset _DEFAULT_ABI_SAVED; fi; if [[ ${ABI} != ${DEFAULT_ABI} ]]; then for v in "${save_restore_variables[@]}"; do vv="_abi_saved_${v}"; [[ ${!v+set} == "set" ]] && export ${vv}="${!v}" || unset ${vv}; done; export _DEFAULT_ABI_SAVED="true"; if [[ ${CBUILD} == "${CHOST}" ]]; then export CBUILD=$(get_abi_CHOST $1); fi; export CHOST=$(get_abi_CHOST ${DEFAULT_ABI}); export AR="$(tc-getAR)"; export CC="$(tc-getCC) $(get_abi_CFLAGS)"; export CXX="$(tc-getCXX) $(get_abi_CFLAGS)"; export F77="$(tc-getF77) $(get_abi_CFLAGS)"; export FC="$(tc-getFC) $(get_abi_CFLAGS)"; export LD="$(tc-getLD) $(get_abi_LDFLAGS)"; export NM="$(tc-getNM)"; export OBJCOPY="$(tc-getOBJCOPY)"; export OBJDUMP="$(tc-getOBJDUMP)"; export PKG_CONFIG="$(tc-getPKG_CONFIG)"; export RANLIB="$(tc-getRANLIB)"; export READELF="$(tc-getREADELF)"; export STRINGS="$(tc-getSTRINGS)"; export STRIP="$(tc-getSTRIP)"; export CHOST=$(get_abi_CHOST $1); export PKG_CONFIG_LIBDIR=${EPREFIX}/usr/$(get_libdir)/pkgconfig; export PKG_CONFIG_PATH=${EPREFIX}/usr/share/pkgconfig; export PKG_CONFIG_SYSTEM_INCLUDE_PATH=${EPREFIX}/usr/include; export PKG_CONFIG_SYSTEM_LIBRARY_PATH=${EPREFIX}/$(get_libdir):${EPREFIX}/usr/$(get_libdir); fi } no-as-needed () { [[ $# -ne 0 ]] && die "no-as-needed takes no arguments"; case $($(tc-getLD) -v 2>&1 < /dev/null) in *GNU*) echo "-Wl,--no-as-needed" ;; esac } number_abis () { set -- `get_install_abis`; echo $# } pkg_nofetch () { default } pkg_postinst () { linux-mod-r1_pkg_postinst "$@" } pkg_setup () { CONFIG_CHECK=" INET NET NET_UDP_TUNNEL DST_CACHE CRYPTO CRYPTO_AES CRYPTO_GCM CRYPTO_CHACHA20POLY1305"; linux-mod-r1_pkg_setup } post_src_install () { ( if grep -E -q 'internal compiler error' "${WORKDIR}"/*/config.log &> /dev/null; then echo "${CATEGORY}/${PF}: Found ICE in config.log?!"; fi; if [[ -f "${S}"/meson.build ]] && ! grep -q "dev-util/meson" <<< "${BDEPEND}"; then echo "${CATEGORY}/${PF}: meson.build found but ebuild doesn't use meson?"; fi; if grep -r -q "dejagnu" "${S}" &> /dev/null && ! grep -q "dejagnu" <<< "${BDEPEND}"; then echo "${CATEGORY}/${PF}: Missing dejagnu tests?"; fi; if grep -r -q "test" "${S}/meson_options.txt" &> /dev/null && ! grep -q "test" <<< "${IUSE}"; then echo "${CATEGORY}/${PF}: Missing test option wiring for meson?"; fi; if grep -E -r -q -- "(disable|enable|with(out)?)-(unit)?test(s?)" configure.ac &> /dev/null && ! grep -q "test" <<< "${IUSE}"; then echo "${CATEGORY}/${PF}: Missing test option wiring for autoconf?"; fi; if grep -E -r -q -- "(disable|enable)-valgrind" configure.ac &> /dev/null && ! grep -q "valgrind" <<< "${IUSE}"; then echo "${CATEGORY}/${PF}: Missing valgrind option wiring for autoconf?"; fi; if grep -r -q "valgrind" "${S}/meson_options.txt" &> /dev/null && ! grep -q "valgrind" <<< "${IUSE}"; then echo "${CATEGORY}/${PF}: Missing valgrind option wiring for meson?"; fi; if grep -E -r -q -- "(disable|enable)-fuzz" configure.ac &> /dev/null && ! grep -q "fuzz" <<< "${EBUILD}"; then echo "${CATEGORY}/${PF}: Missing fuzz option wiring for autoconf?"; fi; if grep -r -q "fuzz" "${S}/meson_options.txt" &> /dev/null && ! grep -q "fuzz" <<< "${EBUILD}"; then echo "${CATEGORY}/${PF}: Missing fuzz option wiring for meson?"; fi ) &>> /var/tmp/sam.txt } qeerror () { qout eerror "${@}" } qeinfo () { qout einfo "${@}" } qewarn () { qout ewarn "${@}" } qout () { local outputmsg type; type=${1}; shift; outputmsg="${@}"; case "${EBUILD_PHASE}" in depend) unset outputmsg ;; clean) unset outputmsg ;; preinst) unset outputmsg ;; esac; [[ -n "${outputmsg}" ]] && ${type} "${outputmsg}" } raw-ldflags () { local x input="$@"; [[ -z ${input} ]] && input=${LDFLAGS}; set --; for x in ${input}; do case ${x} in -Wl,*) x=${x#-Wl,}; set -- "$@" ${x//,/ } ;; *) ;; esac; done; echo "$@" } replace-cpu-flags () { local newcpu="$#"; newcpu="${!newcpu}"; while [ $# -gt 1 ]; do replace-flags "-march=${1}" "-march=${newcpu}"; replace-flags "-mcpu=${1}" "-mcpu=${newcpu}"; replace-flags "-mtune=${1}" "-mtune=${newcpu}"; shift; done; return 0 } replace-flags () { [[ $# != 2 ]] && die "Usage: replace-flags "; local f var new; for var in $(all-flag-vars); do new=(); for f in ${!var}; do [[ ${f} == ${1} ]] && f=${2}; new+=("${f}"); done; export ${var}="${new[*]}"; done; return 0 } replace-sparc64-flags () { [[ $# -ne 0 ]] && die "replace-sparc64-flags takes no arguments"; local SPARC64_CPUS="ultrasparc3 ultrasparc v9"; if [ "${CFLAGS/mtune}" != "${CFLAGS}" ]; then for x in ${SPARC64_CPUS}; do CFLAGS="${CFLAGS/-mcpu=${x}/-mcpu=v8}"; done; else for x in ${SPARC64_CPUS}; do CFLAGS="${CFLAGS/-mcpu=${x}/-mcpu=v8 -mtune=${x}}"; done; fi; if [ "${CXXFLAGS/mtune}" != "${CXXFLAGS}" ]; then for x in ${SPARC64_CPUS}; do CXXFLAGS="${CXXFLAGS/-mcpu=${x}/-mcpu=v8}"; done; else for x in ${SPARC64_CPUS}; do CXXFLAGS="${CXXFLAGS/-mcpu=${x}/-mcpu=v8 -mtune=${x}}"; done; fi; export CFLAGS CXXFLAGS } require_configured_kernel () { [[ -n ${SKIP_KERNEL_CHECK} ]] && return; if ! use kernel_linux; then die "${FUNCNAME}() called on non-Linux system, please fix the ebuild"; fi; if ! linux_config_src_exists; then qeerror "Could not find a usable .config in the kernel source directory."; qeerror "Please ensure that ${KERNEL_DIR} points to a configured set of Linux sources."; qeerror "If you are using KBUILD_OUTPUT, please set the environment var so that"; qeerror "it points to the necessary object directory so that it might find .config."; die "Kernel not configured; no .config found in ${KV_OUT_DIR}"; fi; get_version || die "Unable to determine configured kernel version" } set_arch_to_kernel () { export ARCH=$(tc-arch-kernel) } set_arch_to_pkgmgr () { export ARCH=$(tc-arch) } setup-allowed-flags () { [[ ${EAPI} == [67] ]] || die "Internal function ${FUNCNAME} is not available in EAPI ${EAPI}."; _setup-allowed-flags "$@" } source_profile () { set +u; source /etc/profile 2> /dev/null; set -u } declare -fx source_profile src_compile () { local modlist=("ovpn-dco-v2=updates:.:drivers/net/ovpn-dco"); local modargs=(KERNEL_SRC="${KERNEL_DIR}"); [[ ${PV} != 9999 ]] && modargs+=(REVISION="${PV}"); use debug && modargs+=(DEBUG=1); linux-mod-r1_src_compile } src_configure () { filter-flags -fomit-frame-pointer; default } src_install () { linux-mod-r1_src_install; insinto /usr/share/${PN}; doins -r include } src_prepare () { default } src_test () { default } src_unpack () { default } strip-flags () { [[ $# -ne 0 ]] && die "strip-flags takes no arguments"; local x y var; local ALLOWED_FLAGS; _setup-allowed-flags; set -f; for var in $(all-flag-vars); do local new=(); for x in ${!var}; do for y in "${ALLOWED_FLAGS[@]}"; do if [[ ${x} == ${y} ]]; then new+=("${x}"); break; fi; done; done; if _is_flagq ${var} "-O*" && ! _is_flagq new "-O*"; then new+=(-O2); fi; if [[ ${!var} != "${new[*]}" ]]; then einfo "strip-flags: ${var}: changed '${!var}' to '${new[*]}'"; fi; export ${var}="${new[*]}"; done; set +f; return 0 } strip-unsupported-flags () { [[ $# -ne 0 ]] && die "strip-unsupported-flags takes no arguments"; export CFLAGS=$(test-flags-CC ${CFLAGS}); export CXXFLAGS=$(test-flags-CXX ${CXXFLAGS}); export FFLAGS=$(test-flags-F77 ${FFLAGS}); export FCFLAGS=$(test-flags-FC ${FCFLAGS}); export LDFLAGS=$(test-flags-CCLD ${LDFLAGS}) } syncRepo () { cd /var/db/repos/gentoo; local synclog=/var/tmp/tb/sync.log; local curr_time=$EPOCHSECONDS; if ! emaint sync --auto &> $synclog; then if grep -q -e 'git fetch error' -e ': Failed to connect to ' -e ': SSL connection timeout' -e ': Connection timed out' -e 'The requested URL returned error:' $synclog; then return 0; fi; ReachedEOL "broken ::gentoo" $synclog; fi; if grep -q -F '* An update to portage is available.' $synclog; then add2backlog "sys-apps/portage"; fi; if ! grep -B 1 '=== Sync completed for gentoo' $synclog | grep -q 'Already up to date.'; then git diff --diff-filter="ACM" --name-only "@{ $((EPOCHSECONDS - last_sync + 3600)) second ago }..@{ 1 hour ago }" 2> /dev/null | grep -F -e '/files/' -e '.ebuild' -e 'Manifest' | cut -f 1-2 -d '/' -s | grep -v -f /mnt/tb/data/IGNORE_PACKAGES | sort -u > /tmp/syncRepo.upd; if [[ -s /tmp/syncRepo.upd ]]; then sort -u /tmp/syncRepo.upd /var/tmp/tb/backlog.upd | shuf > /tmp/backlog.upd; cp /tmp/backlog.upd /var/tmp/tb/backlog.upd; fi; fi; last_sync=$curr_time; cd - > /dev/null } declare -fx syncRepo tc-arch () { tc-ninja_magic_to_arch portage "$@" } tc-arch-kernel () { tc-ninja_magic_to_arch kern "$@" } tc-check-openmp () { if ! _tc-has-openmp; then eerror "Your current compiler does not support OpenMP!"; if tc-is-gcc; then eerror "Enable OpenMP support by building sys-devel/gcc with USE=\"openmp\"."; else if tc-is-clang; then eerror "OpenMP support in sys-devel/clang is provided by sys-libs/libomp."; fi; fi; die "Active compiler does not have required support for OpenMP"; fi } tc-cpp-is-true () { local CONDITION=${1}; shift; $(tc-getTARGET_CPP) "${@}" -P - <<-EOF > /dev/null 2>&1 #if ${CONDITION} true #else #error false #endif EOF } tc-detect-is-softfloat () { [[ $(tc-getTARGET_CPP) == "gcc -E" ]] && return 1; case ${CTARGET:-${CHOST}} in *-newlib | *-elf | *-eabi) return 1 ;; arm*) if tc-cpp-is-true "defined(__ARM_PCS_VFP)"; then echo "no"; else if tc-cpp-is-true "defined(__SOFTFP__)"; then echo "yes"; else echo "softfp"; fi; fi; return 0 ;; *) return 1 ;; esac } tc-enables-cxx-assertions () { tc-cpp-is-true "defined(_GLIBCXX_ASSERTIONS) || defined(_LIBCPP_ENABLE_ASSERTIONS)" ${CPPFLAGS} ${CXXFLAGS} } tc-enables-fortify-source () { tc-cpp-is-true "defined(_FORTIFY_SOURCE)" ${CPPFLAGS} ${CFLAGS} ${CXXFLAGS} } tc-enables-pie () { tc-cpp-is-true "defined(__PIE__)" ${CPPFLAGS} ${CFLAGS} ${CXXFLAGS} } tc-enables-ssp () { tc-cpp-is-true "defined(__SSP__) || defined(__SSP_STRONG__) || defined(__SSP_ALL__)" ${CPPFLAGS} ${CFLAGS} ${CXXFLAGS} } tc-enables-ssp-all () { tc-cpp-is-true "defined(__SSP_ALL__)" ${CPPFLAGS} ${CFLAGS} ${CXXFLAGS} } tc-enables-ssp-strong () { tc-cpp-is-true "defined(__SSP_STRONG__) || defined(__SSP_ALL__)" ${CPPFLAGS} ${CFLAGS} ${CXXFLAGS} } tc-endian () { local host=$1; [[ -z ${host} ]] && host=${CTARGET:-${CHOST}}; host=${host%%-*}; case ${host} in aarch64*be) echo big ;; aarch64) echo little ;; alpha*) echo little ;; arm*b*) echo big ;; arm*) echo little ;; cris*) echo little ;; hppa*) echo big ;; i?86*) echo little ;; ia64*) echo little ;; loongarch*) echo little ;; m68*) echo big ;; mips*l*) echo little ;; mips*) echo big ;; powerpc*le) echo little ;; powerpc*) echo big ;; riscv*) echo little ;; s390*) echo big ;; sh*b*) echo big ;; sh*) echo little ;; sparc*) echo big ;; x86_64*) echo little ;; *) echo wtf ;; esac } tc-env_build () { tc-export_build_env; CFLAGS=${BUILD_CFLAGS} CXXFLAGS=${BUILD_CXXFLAGS} CPPFLAGS=${BUILD_CPPFLAGS} LDFLAGS=${BUILD_LDFLAGS} AR=$(tc-getBUILD_AR) AS=$(tc-getBUILD_AS) CC=$(tc-getBUILD_CC) CPP=$(tc-getBUILD_CPP) CXX=$(tc-getBUILD_CXX) LD=$(tc-getBUILD_LD) NM=$(tc-getBUILD_NM) PKG_CONFIG=$(tc-getBUILD_PKG_CONFIG) RANLIB=$(tc-getBUILD_RANLIB) READELF=$(tc-getBUILD_READELF) "$@" } tc-export () { local var; for var in "$@"; do [[ $(type -t "tc-get${var}") != "function" ]] && die "tc-export: invalid export variable '${var}'"; "tc-get${var}" > /dev/null; done } tc-export_build_env () { tc-export "$@"; if tc-is-cross-compiler; then : "${BUILD_CFLAGS:=-O1 -pipe}"; : "${BUILD_CXXFLAGS:=-O1 -pipe}"; : "${BUILD_CPPFLAGS:= }"; : "${BUILD_LDFLAGS:= }"; else : "${BUILD_CFLAGS:=${CFLAGS}}"; : "${BUILD_CXXFLAGS:=${CXXFLAGS}}"; : "${BUILD_CPPFLAGS:=${CPPFLAGS}}"; : "${BUILD_LDFLAGS:=${LDFLAGS}}"; fi; export BUILD_{C,CXX,CPP,LD}FLAGS; local v; for v in BUILD_{C,CXX,CPP,LD}FLAGS; do export ${v#BUILD_}_FOR_BUILD="${!v}"; done } tc-get-c-rtlib () { local res=$($(tc-getCC) ${CPPFLAGS} ${CFLAGS} ${LDFLAGS} -print-libgcc-file-name 2> /dev/null); case ${res} in *libclang_rt*) echo compiler-rt ;; *libgcc*) echo libgcc ;; *) return 1 ;; esac; return 0 } tc-get-compiler-type () { local code=' #if defined(__PATHSCALE__) HAVE_PATHCC #elif defined(__clang__) HAVE_CLANG #elif defined(__GNUC__) HAVE_GCC #endif '; local res=$($(tc-getCPP "$@") -E -P - <<< "${code}"); case ${res} in *HAVE_PATHCC*) echo pathcc ;; *HAVE_CLANG*) echo clang ;; *HAVE_GCC*) echo gcc ;; *) echo unknown ;; esac } tc-get-cxx-stdlib () { local code='#include #if defined(_LIBCPP_VERSION) HAVE_LIBCXX #elif defined(__GLIBCXX__) HAVE_LIBSTDCPP #endif '; local res=$($(tc-getCXX) ${CPPFLAGS} ${CXXFLAGS} -x c++ -E -P - <<< "${code}" 2> /dev/null); case ${res} in *HAVE_LIBCXX*) echo libc++ ;; *HAVE_LIBSTDCPP*) echo libstdc++ ;; *) return 1 ;; esac; return 0 } tc-getAR () { tc-getPROG AR ar "$@" } tc-getAS () { tc-getPROG AS as "$@" } tc-getBUILD_AR () { tc-getBUILD_PROG AR ar "$@" } tc-getBUILD_AS () { tc-getBUILD_PROG AS as "$@" } tc-getBUILD_CC () { tc-getBUILD_PROG CC gcc "$@" } tc-getBUILD_CPP () { tc-getBUILD_PROG CPP "$(tc-getBUILD_CC) -E" "$@" } tc-getBUILD_CXX () { tc-getBUILD_PROG CXX g++ "$@" } tc-getBUILD_LD () { tc-getBUILD_PROG LD ld "$@" } tc-getBUILD_NM () { tc-getBUILD_PROG NM nm "$@" } tc-getBUILD_OBJCOPY () { tc-getBUILD_PROG OBJCOPY objcopy "$@" } tc-getBUILD_PKG_CONFIG () { tc-getBUILD_PROG PKG_CONFIG pkg-config "$@" } tc-getBUILD_PROG () { local vars="BUILD_$1 $1_FOR_BUILD HOST$1"; tc-is-cross-compiler || vars+=" $1"; _tc-getPROG CBUILD "${vars}" "${@:2}" } tc-getBUILD_RANLIB () { tc-getBUILD_PROG RANLIB ranlib "$@" } tc-getBUILD_READELF () { tc-getBUILD_PROG READELF readelf "$@" } tc-getBUILD_STRINGS () { tc-getBUILD_PROG STRINGS strings "$@" } tc-getBUILD_STRIP () { tc-getBUILD_PROG STRIP strip "$@" } tc-getCC () { tc-getPROG CC gcc "$@" } tc-getCPP () { tc-getPROG CPP "${CC:-gcc} -E" "$@" } tc-getCXX () { tc-getPROG CXX g++ "$@" } tc-getDLLWRAP () { tc-getPROG DLLWRAP dllwrap "$@" } tc-getF77 () { tc-getPROG F77 gfortran "$@" } tc-getFC () { tc-getPROG FC gfortran "$@" } tc-getGCJ () { tc-getPROG GCJ gcj "$@" } tc-getGO () { tc-getPROG GO gccgo "$@" } tc-getLD () { tc-getPROG LD ld "$@" } tc-getNM () { tc-getPROG NM nm "$@" } tc-getOBJCOPY () { tc-getPROG OBJCOPY objcopy "$@" } tc-getOBJDUMP () { tc-getPROG OBJDUMP objdump "$@" } tc-getPKG_CONFIG () { tc-getPROG PKG_CONFIG pkg-config "$@" } tc-getPROG () { _tc-getPROG CHOST "$@" } tc-getRANLIB () { tc-getPROG RANLIB ranlib "$@" } tc-getRC () { tc-getPROG RC windres "$@" } tc-getREADELF () { tc-getPROG READELF readelf "$@" } tc-getSTRINGS () { tc-getPROG STRINGS strings "$@" } tc-getSTRIP () { tc-getPROG STRIP strip "$@" } tc-getTARGET_CPP () { if [[ -n ${CTARGET} ]]; then _tc-getPROG CTARGET TARGET_CPP "gcc -E" "$@"; else tc-getCPP "$@"; fi } tc-has-tls () { local base="${T}/test-tc-tls"; cat <<-EOF > "${base}.c" int foo(int *i) { static __thread int j = 0; return *i ? j : *i; } EOF local flags; case $1 in -s) flags="-S" ;; -c) flags="-c" ;; -l) ;; -*) die "Usage: tc-has-tls [-c|-l] [toolchain prefix]" ;; esac; : "${flags:=-fPIC -shared -Wl,-z,defs}"; [[ $1 == -* ]] && shift; $(tc-getCC "$@") ${flags} "${base}.c" -o "${base}" >&/dev/null; local ret=$?; rm -f "${base}"*; return ${ret} } tc-is-clang () { [[ $(tc-get-compiler-type) == clang ]] } tc-is-cross-compiler () { [[ ${CBUILD:-${CHOST}} != ${CHOST} ]] } tc-is-gcc () { [[ $(tc-get-compiler-type) == gcc ]] } tc-is-softfloat () { tc-detect-is-softfloat || tc-tuple-is-softfloat } tc-is-static-only () { local host=${CTARGET:-${CHOST}}; [[ ${host} == *-mint* ]] } tc-ld-disable-gold () { tc-ld-is-gold "$@" && tc-ld-force-bfd "$@" } tc-ld-force-bfd () { if ! tc-ld-is-gold "$@" && ! tc-ld-is-lld "$@"; then return; fi; ewarn "Forcing usage of the BFD linker"; local ld=$(tc-getLD "$@"); local bfd_ld="${ld%% *}.bfd"; local path_ld=$(type -P "${bfd_ld}" 2> /dev/null); [[ -e ${path_ld} ]] && export LD=${bfd_ld}; if tc-is-gcc || tc-is-clang; then export LDFLAGS="${LDFLAGS} -fuse-ld=bfd"; fi } tc-ld-is-gold () { local out; local -x LC_ALL=C; out=$($(tc-getLD "$@") --version 2>&1); if [[ ${out} == *"GNU gold"* ]]; then return 0; fi; local base="${T}/test-tc-gold"; cat <<-EOF > "${base}.c" int main(void) { return 0; } EOF out=$($(tc-getCC "$@") ${CFLAGS} ${CPPFLAGS} ${LDFLAGS} -Wl,--version "${base}.c" -o "${base}" 2>&1); rm -f "${base}"*; if [[ ${out} == *"GNU gold"* ]]; then return 0; fi; return 1 } tc-ld-is-lld () { local out; local -x LC_ALL=C; out=$($(tc-getLD "$@") --version 2>&1); if [[ ${out} == *"LLD"* ]]; then return 0; fi; local base="${T}/test-tc-lld"; cat <<-EOF > "${base}.c" int main(void) { return 0; } EOF out=$($(tc-getCC "$@") ${CFLAGS} ${CPPFLAGS} ${LDFLAGS} -Wl,--version "${base}.c" -o "${base}" 2>&1); rm -f "${base}"*; if [[ ${out} == *"LLD"* ]]; then return 0; fi; return 1 } tc-ninja_magic_to_arch () { function _tc_echo_kernel_alias () { [[ ${type} == "kern" ]] && echo $1 || echo $2 }; local type=$1; local host=$2; [[ -z ${host} ]] && host=${CTARGET:-${CHOST}}; case ${host} in aarch64*) echo arm64 ;; alpha*) echo alpha ;; arm*) echo arm ;; avr*) _tc_echo_kernel_alias avr32 avr ;; bfin*) _tc_echo_kernel_alias blackfin bfin ;; c6x*) echo c6x ;; cris*) echo cris ;; frv*) echo frv ;; hexagon*) echo hexagon ;; hppa*) _tc_echo_kernel_alias parisc hppa ;; i?86*) echo x86 ;; ia64*) echo ia64 ;; loongarch*) _tc_echo_kernel_alias loongarch loong ;; m68*) echo m68k ;; metag*) echo metag ;; microblaze*) echo microblaze ;; mips*) echo mips ;; nios2*) echo nios2 ;; nios*) echo nios ;; or1k* | or32*) echo openrisc ;; powerpc*) if [[ ${type} == "kern" ]]; then echo powerpc; else if [[ ${host} == powerpc64* ]]; then echo ppc64; else echo ppc; fi; fi ;; riscv*) echo riscv ;; s390*) echo s390 ;; score*) echo score ;; sh64*) _tc_echo_kernel_alias sh64 sh ;; sh*) echo sh ;; sparc64*) _tc_echo_kernel_alias sparc64 sparc ;; sparc*) [[ ${PROFILE_ARCH} == "sparc64" ]] && _tc_echo_kernel_alias sparc64 sparc || echo sparc ;; tile*) echo tile ;; vax*) echo vax ;; x86_64*) if [[ ${type} == "kern" ]]; then echo x86; else echo amd64; fi ;; xtensa*) echo xtensa ;; *) echo unknown ;; esac } tc-stack-grows-down () { case ${ARCH} in hppa | metag) return 1 ;; esac; return 0 } tc-tuple-is-softfloat () { local CTARGET=${CTARGET:-${CHOST}}; case ${CTARGET//_/-} in bfin* | h8300*) echo "only" ;; *-softfloat-*) echo "yes" ;; *-softfp-*) echo "softfp" ;; arm*-hardfloat-* | arm*eabihf) echo "no" ;; *-newlib | *-elf | *-eabi) echo "no" ;; arm*) echo "yes" ;; *) echo "no" ;; esac } test-compile () { local lang=$1; local code=$2; shift 2; [[ -z "${lang}" ]] && return 1; [[ -z "${code}" ]] && return 1; local compiler filename_in filename_out args=() libs=(); case "${lang}" in c) compiler="$(tc-getCC)"; filename_in="${T}/test.c"; filename_out="${T}/test.o"; args+=(${CFLAGS[@]} -xc -c) ;; c++) compiler="$(tc-getCXX)"; filename_in="${T}/test.cc"; filename_out="${T}/test.o"; args+=(${CXXFLAGS[@]} -xc++ -c) ;; f77) compiler="$(tc-getF77)"; filename_in="${T}/test.f"; filename_out="${T}/test.o"; args+=(${FFFLAGS[@]} -xf77 -c) ;; f95) compiler="$(tc-getFC)"; filename_in="${T}/test.f90"; filename_out="${T}/test.o"; args+=(${FCFLAGS[@]} -xf95 -c) ;; c+ld) compiler="$(tc-getCC)"; filename_in="${T}/test.c"; filename_out="${T}/test.exe"; args+=(${CFLAGS[@]} ${LDFLAGS[@]} -xc); libs+=(${LIBS[@]}) ;; c+++ld) compiler="$(tc-getCXX)"; filename_in="${T}/test.cc"; filename_out="${T}/test.exe"; args+=(${CXXFLAGS[@]} ${LDFLAGS[@]} -xc++); libs+=(${LIBS[@]}) ;; f77+ld) compiler="$(tc-getF77)"; filename_in="${T}/test.f"; filename_out="${T}/test.exe"; args+=(${FFLAGS[@]} ${LDFLAGS[@]} -xf77); libs+=(${LIBS[@]}) ;; f95+ld) compiler="$(tc-getFC)"; filename_in="${T}/test.f90"; filename_out="${T}/test.exe"; args+=(${FCFLAGS[@]} ${LDFLAGS[@]} -xf95); libs+=(${LIBS[@]}) ;; *) die "Unknown compiled language ${lang}" ;; esac; printf "%s\n" "${code}" > "${filename_in}" || die "Failed to create '${test_in}'"; "${compiler}" ${args[@]} "${filename_in}" -o "${filename_out}" ${libs[@]} &> /dev/null } test-flag-CC () { _test-flag-PROG CC c "$@" } test-flag-CCLD () { _test-flag-PROG CC c+ld "$@" } test-flag-CXX () { _test-flag-PROG CXX c++ "$@" } test-flag-F77 () { _test-flag-PROG F77 f77 "$@" } test-flag-FC () { _test-flag-PROG FC f95 "$@" } test-flag-PROG () { [[ ${EAPI} == [67] ]] || die "Internal function ${FUNCNAME} is not available in EAPI ${EAPI}."; _test-flag-PROG "$@" } test-flags () { test-flags-CC "$@" } test-flags-CC () { _test-flags-PROG CC "$@" } test-flags-CCLD () { _test-flags-PROG CCLD "$@" } test-flags-CXX () { _test-flags-PROG CXX "$@" } test-flags-F77 () { _test-flags-PROG F77 "$@" } test-flags-FC () { _test-flags-PROG FC "$@" } test-flags-PROG () { [[ ${EAPI} == [67] ]] || die "Internal function ${FUNCNAME} is not available in EAPI ${EAPI}."; _test-flags-PROG "$@" } test_version_info () { if [[ $($(tc-getCC) --version 2>&1) == *$1* ]]; then return 0; else return 1; fi } ver_cut () { local range=${1}; local v=${2:-${PV}}; local start end; local -a comp; __eapi7_ver_split "${v}"; local max=$((${#comp[@]}/2)); __eapi7_ver_parse_range "${range}" "${max}"; local IFS=; if [[ ${start} -gt 0 ]]; then start=$(( start*2 - 1 )); fi; echo "${comp[*]:start:end*2-start}" } ver_rs () { local v; (( ${#} & 1 )) && v=${@: -1} || v=${PV}; local start end i; local -a comp; __eapi7_ver_split "${v}"; local max=$((${#comp[@]}/2 - 1)); while [[ ${#} -ge 2 ]]; do __eapi7_ver_parse_range "${1}" "${max}"; for ((i = start*2; i <= end*2; i+=2 )) do [[ ${i} -eq 0 && -z ${comp[i]} ]] && continue; comp[i]=${2}; done; shift 2; done; local IFS=; echo "${comp[*]}" } ver_test () { local va op vb; if [[ $# -eq 3 ]]; then va=${1}; shift; else va=${PVR}; fi; [[ $# -eq 2 ]] || die "${FUNCNAME}: bad number of arguments"; op=${1}; vb=${2}; case ${op} in -eq | -ne | -lt | -le | -gt | -ge) ;; *) die "${FUNCNAME}: invalid operator: ${op}" ;; esac; __eapi7_ver_compare "${va}" "${vb}"; test $? "${op}" 2 }