environment

environment (text/plain), 142.05 KB, created by Toralf Förster on 2024-08-28 17:24:40 UTC

declare -x ABI="amd64"
declare -x ABI_MIPS=""
declare -x ABI_S390=""
declare -x ABI_X86="64"
declare -x ADA_TARGET=""
declare -x ADDR2LINE="llvm-addr2line"
declare -x ALLOW_TEST="network"
declare -x ALSA_CARDS=""
declare -x AMDGPU_TARGETS=""
declare -x APACHE2_MODULES=""
declare -x APACHE2_MPMS=""
declare -x AR="llvm-ar"
declare -x ARCH="amd64"
declare -x AS="clang -c"
declare BDEPEND=$'\n\t \n\tsys-apps/kmod[tools]\n\tmodules-sign? (\n\t\tdev-libs/openssl\n\t\tvirtual/pkgconfig\n\t)\n virtual/pkgconfig'
declare -x BINPKG_FORMAT="gpkg"
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 pkg-config split-usr xml python_targets_python3_12 python_single_target_python3_12 gil multilib zstd cet ssl curl_ssl_openssl -binutils-plugin compiler-rt clang libunwind default-compiler-rt default-lld default-libcxx llvm-libunwind libcxx -sanitize libcxxabi -llvm_targets_BPF -llvm_targets_AMDGPU -llvm_targets_NVPTX -llvm_targets_BPF"
declare -x CALLIGRA_FEATURES=""
declare -x CAMERAS=""
declare -x CARGO_TERM_COLOR="never"
declare -x CBUILD="x86_64-pc-linux-gnu"
declare -x CC="clang"
declare -x CCL_DEFAULT_DIRECTORY="/usr/lib64/clozurecl"
declare -x CFLAGS="-O2 -pipe -march=native -fno-diagnostics-color -Werror=implicit-function-declaration -Werror=implicit-int"
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="~MAC80211 ~BT_HCIBTUSB"
declare -x CPP="clang-cpp"
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_QUIC=""
declare -x CURL_SSL=""
declare -x CXX="clang++"
declare -x CXXFLAGS="-O2 -pipe -march=native -fno-diagnostics-color"
declare -x CXXSTDLIB="c++"
declare -x DEFAULT_ABI="amd64"
declare -x DEFINED_PHASES=" compile install postinst postrm setup unpack"
declare DEPEND=$'\n\tvirtual/linux-sources\n'
declare DESCRIPTION="aic8800 driver for AICSemi AIC8800/8801/8800DC/8800DW/8800FC Wifi/Bluetooth"
declare -x DIROPTIONS="-m0755"
declare -x EAPI="8"
declare -x EGO_BUILD_FLAGS="-p 4"
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="1724836836.275411"
declare -- EPOCHSECONDS="1724836836"
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="4"
declare -x GPG_VERIFY_GROUP_DROP="nogroup"
declare -x GPG_VERIFY_USER_DROP="nobody"
declare -x GPSD_PROTOCOLS=""
declare -x GRUB_PLATFORMS=""
declare -x GUILE_SINGLE_TARGET=""
declare -x GUILE_TARGETS=""
declare HOMEPAGE="https://www.aicsemi.com/ https://linux.brostrend.com/troubleshooting/source-code/"
declare IDEPEND=$'\n\tsys-apps/kmod[tools]\n'
declare -x INHERITED=" mount-boot-utils toolchain-funcs multilib dist-kernel-utils edo linux-info multiprocessing linux-mod-r1 udev unpacker"
declare -x INPUT_DEVICES=""
declare -x INSOPTIONS="-m0644"
declare IUSE="+firmware udev dist-kernel modules-compress modules-sign +strip "
declare -x IUSE_EFFECTIVE="abi_x86_64 alpha amd64 amd64-linux arm arm64 arm64-macos dist-kernel elibc_Darwin elibc_SunOS elibc_bionic elibc_glibc elibc_mingw elibc_musl firmware hppa ia64 kernel_Darwin kernel_SunOS kernel_linux loong m68k mips modules-compress modules-sign ppc ppc-macos ppc64 ppc64-linux prefix prefix-guest prefix-stack riscv s390 sparc strip udev 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/lib/llvm/18/bin/x86_64-pc-linux-gnu-ar"
declare -- KERNEL_CC="/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-clang-18"
declare -- KERNEL_CHOST="x86_64-pc-linux-gnu"
declare -- KERNEL_CXX="/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-clang++-18"
declare -- KERNEL_DIR="/usr/src/linux"
declare -- KERNEL_LD="/usr/lib/llvm/18/bin/ld.lld"
declare -- KERNEL_MAKEFILE="/usr/src/linux/Makefile"
declare -- KERNEL_NM="/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-nm"
declare -- KERNEL_OBJCOPY="/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-objcopy"
declare -- KERNEL_OBJDUMP="/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-objdump"
declare -- KERNEL_READELF="/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-readelf"
declare -- KERNEL_STRIP="/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-strip"
declare -x KEYWORDS="~amd64"
declare -- KV_DIR="/usr/src/linux"
declare -- KV_EXTRA=""
declare -- KV_FULL="6.10.6-gentoo-dist"
declare -- KV_LOCAL="-gentoo-dist"
declare -- KV_MAJOR="6"
declare -- KV_MINOR="10"
declare -- KV_OUT_DIR="/usr/src/linux"
declare -- KV_PATCH="6"
declare -x L10N=""
declare -x LADSPA_PATH="/usr/lib64/ladspa"
declare -x LANG="C.UTF8"
declare -x LCD_DEVICES=""
declare -x LC_COLLATE="C"
declare -x LC_MESSAGES="C"
declare -x LD="ld.lld"
declare -x LDFLAGS="-Wl,-O1 -Wl,--as-needed -Wl,-z,pack-relative-relocs -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+ firmware? ( freedist )"
declare -x LINUX_CONFIG_EXISTS_DONE="1"
declare -x LLVM_SLOT=""
declare -x LLVM_TARGETS=""
declare -x LLVM_USE_LIBCXX="1"
declare -x LOGTALKHOME="/usr/share/logtalk-3.47.0"
declare -x LUA_SINGLE_TARGET=""
declare -x LUA_TARGETS=""
declare -x MAILTO="tinderbox"
declare -x MAKEOPTS=" -j4"
declare -x MANPAGER="manpager"
declare -x MIX_REBAR3="/usr/bin/rebar3"
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=true" [9]="STRIP=true" [10]="CROSS_COMPILE=x86_64-pc-linux-gnu-" [11]="HOSTCC=clang" [12]="HOSTCXX=clang++" [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,-z,pack-relative-relocs -Wl,--as-needed -Wl,--defsym=__gentoo_check_ldflags__=0" [16]="HOSTPKG_CONFIG=x86_64-pc-linux-gnu-pkg-config" [17]="CC=/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-clang-18" [18]="CXX=/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-clang++-18" [19]="LD=/usr/lib/llvm/18/bin/ld.lld" [20]="AR=/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-ar" [21]="NM=/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-nm" [22]="OBJCOPY=/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-objcopy" [23]="OBJDUMP=/usr/lib/llvm/18/bin/x86_64-pc-linux-gnu-objdump" [24]="READELF=/usr/lib/llvm/18/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 NM="llvm-nm"
declare -x NPM_CONFIG_GLOBALCONFIG="/etc/npm/npmrc"
declare -x OBJCOPY="llvm-objcopy"
declare -x OBJDUMP="llvm-objdump"
declare -x OCAML_COLOR="never"
declare -x OFFICE_IMPLEMENTATION=""
declare -x OMP_DYNAMIC="FALSE"
declare -x OMP_NESTED="FALSE"
declare -x OMP_NUM_THREADS="4"
declare -x OPENMPI_FABRICS=""
declare -x OPENMPI_OFED_FEATURES=""
declare -x OPENMPI_RM=""
declare -x PATH="/var/tmp/portage/net-wireless/aic8800-1.0.5/temp/clang-wrappers:/usr/lib/portage/python3.12/ebuild-helpers/xattr:/usr/lib/portage/python3.12/ebuild-helpers:/usr/local/sbin:/usr/local/bin:/usr/bin:/opt/bin:/usr/lib/llvm/18/bin:/opt/hermes/bin"
declare PDEPEND=""
declare -x PERL_FEATURES=""
declare -x PHP_TARGETS=""
declare -x PKGSYSTEM_ENABLE_FSYNC="0"
declare -x PORTAGE_COMPRESSION_COMMAND="zstd -T4"
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/aic8800-1.0.5/html")
declare -a PORTAGE_DOSTRIP=([0]="/")
declare -a PORTAGE_DOSTRIP_SKIP=()
declare -x PORTAGE_REPO_REVISIONS="{\"gentoo\": \"6702f50aea960a9bcf24a8ccd83fd7f57ac9662f\"}"
declare -- PORTAGE_USE_CLANG_HOOK="1"
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 RANLIB="llvm-ranlib"
declare RDEPEND=$'\n\tsys-apps/kmod[tools]\n\tdist-kernel? ( virtual/dist-kernel:= )\n'
declare -x READELF="llvm-readelf"
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 RUBY_TARGETS=""
declare -x RUST_TEST_TASKS="4"
declare -x RUST_TEST_THREADS="4"
declare -x S="/var/tmp/portage/net-wireless/aic8800-1.0.5/work/usr/src/aic8800-1.0.5"
declare -x SANDBOX_DEBUG="0"
declare -x SANDBOX_DENY=""
declare -x SANDBOX_METHOD="any"
declare -x SANDBOX_PREDICT="/var/tmp/portage/net-wireless/aic8800-1.0.5/homedir:/dev/crypto:/var/cache/man:/dev/random:/proc/self/coredump_filter:/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-wireless/aic8800-1.0.5/homedir/.bash_history"
declare -x SANE_BACKENDS=""
declare -x SE_MANAGER_PATH="/usr/bin/selenium-manager"
declare -x SHELL="/bin/bash"
declare -- SKIP_KERNEL_BINPKG_ENV_RESET="1"
declare -- SKIP_KERNEL_CHECK=""
declare -x SLOT="0"
declare -i SRANDOM="1562883243"
declare SRC_URI="https://linux.brostrend.com/aic8800-dkms.deb -> aic8800-1.0.5.deb"
declare -x STRINGS="llvm-strings"
declare -x STRIP="llvm-strip"
declare -x SYMLINK_LIB="no"
declare -x TERMINFO="/etc/terminfo"
declare -x TWISTED_DISABLE_WRITING_OF_PLUGIN_CACHE="1"
declare -x USE="abi_x86_64 amd64 elibc_glibc firmware kernel_linux strip udev"
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 XTABLES_ADDONS=""
declare -x XZ_OPT="-9 -T4"
declare -- _DIST_KERNEL_UTILS="1"
declare -- _EDO_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 -- _UDEV_ECLASS="1"
declare -- _UNPACKER_ECLASS="1"
declare -x __E_DESTTREE="/usr"
declare -x __E_DOCDESTTREE=""
declare -x __E_EXEDESTTREE=""
declare -x __E_INSDESTTREE=""
declare -- __PORTAGE_HOOK_CLANG="/usr/lib/llvm/18/bin/clang-18"
declare -x ac_cv_c_undeclared_builtin_options="none needed"
declare -x ac_cv_have_decl_strerror_r="yes"
declare -- alias="x86_64-pc-linux-gnu-clang++"
declare -x enable_year2038="no"
declare -- get_version_warning_done=""
declare -x gl_cv_compiler_check_decl_option="-Werror=implicit-function-declaration"
declare -x gl_cv_func_getcwd_path_max="yes"
declare -- hook_timestamp="2023-11-30T22:24"
declare -- hv_args="-b"
declare -x name="23.0_llvm-20240825-084454"
declare -- one_min="24"
declare -- tasks="22"
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 [[ -z $highest ]]; then
        Mail "${FUNCNAME[0]}: cannot get GCC version";
        return;
    fi;
    if ! gcc-config --list-profiles --nocolor | grep -q -F "$highest *"; then
        local current;
        current=$(gcc -dumpversion);
        echo "major version change of gcc: $current -> $highest" | tee -a $taskfile.history;
        gcc-config --nocolor $highest;
        source_profile;
        add2backlog "dev-build/libtool";
        if grep -q '^LIBTOOL="rdlibtool"' /etc/portage/make.conf; then
            add2backlog "dev-build/slibtool";
        fi;
        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
}
__tinderbox_checkEOL () 
{ 
    if [[ -f /var/tmp/tb/EOL || -f /var/tmp/tb/STOP ]]; then
        exit 42;
    fi
}
__tinderbox_loadToHigh () 
{ 
    read -r one_min tasks < <(tr './' ' ' < /proc/loadavg | cut -f 1,7 -d ' ');
    [[ $one_min -ge 32 && $tasks -ge 32 ]]
}
__tinderbox_meson () 
{ 
    ( if grep -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-build/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
}
_clang_fullversion () 
{ 
    local ver="$1";
    shift;
    set -- $($(tc-getCPP "$@") -E -P - <<< "__clang_major__ __clang_minor__ __clang_patchlevel__");
    eval echo "${ver}"
}
_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}"
}
_get_all_makeopts () 
{ 
    echo "${MAKEOPTS} ${GNUMAKEFLAGS} ${MAKEFLAGS}"
}
_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 () 
{ 
    SKIP_KERNEL_BINPKG_ENV_RESET=1;
    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 %q "${@}" --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 () 
{ 
    use modules-compress || return 0;
    local -a compress;
    if linux_chkconfig_present MODULE_COMPRESS_XZ; then
        compress=(xz -q --memlimit-compress=50% --threads="$(makeopts_jobs)" --check=crc32 --lzma2=dict=1MiB);
    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);
            else
                die "USE=modules-compress enabled but no MODULE_COMPRESS* configured";
            fi;
        fi;
    fi;
    einfo "Compressing modules (matching the kernel configuration) ...";
    edob "${compress[@]}" -- "${@}"
}
_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_dracut.conf.d () 
{ 
    ( insinto /usr/lib/dracut/dracut.conf.d;
    [[ -n ${MODULES_INITRAMFS_IUSE} ]] && use ${MODULES_INITRAMFS_IUSE#+} && : add || : omit;
    newins - 10-${PN}.conf <<< "${_}_drivers+=\" ${*%.ko} \"" )
}
_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;
    if use dist-kernel && ! has_version "~virtual/dist-kernel-${KV_MAJOR}.${KV_MINOR}.${KV_PATCH}"; then
        ewarn;
        ewarn "The kernel modules in ${CATEGORY}/${PN} are being built for";
        ewarn "kernel version ${KV_FULL}. But this does not match the";
        ewarn "installed version of virtual/dist-kernel.";
        ewarn;
        ewarn "If this is not intentional, the problem may be corrected by";
        ewarn "using \"eselect kernel\" to set the default kernel version to";
        ewarn "the same version as the installed version of virtual/dist-kernel.";
        ewarn;
        ewarn "If the distribution kernel is being downgraded, ensure that";
        ewarn "virtual/dist-kernel is also downgraded to the same version";
        ewarn "before rebuilding external kernel modules.";
        ewarn;
    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=true STRIP=true);
    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}/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."
}
_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 <omp.h>
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}
}
_udev_get_udevdir () 
{ 
    local -x PKG_CONFIG_FDO_SYSROOT_RULES=1;
    if $($(tc-getPKG_CONFIG) --exists udev); then
        local udevdir="$($(tc-getPKG_CONFIG) --variable=udevdir udev)";
        echo "${udevdir#${EPREFIX}}";
    else
        echo /lib/udev;
    fi
}
_unpacker () 
{ 
    [[ $# -eq 1 ]] || die "Usage: ${FUNCNAME} <file>";
    local a=$1;
    local m=${a,,};
    a=$(find_unpackable_file "${a}");
    local comp=$(_unpacker_get_decompressor "${m}");
    local arch="";
    case ${m} in 
        *.gpkg.tar)
            arch="unpack_gpkg"
        ;;
        *.tgz | *.tbz | *.tbz2 | *.txz | *.tar.* | *.tar)
            arch="tar --no-same-owner -xof"
        ;;
        *.cpio.* | *.cpio)
            arch="unpack_cpio"
        ;;
        *.deb)
            arch="unpack_deb"
        ;;
        *.run)
            arch="unpack_makeself"
        ;;
        *.sh)
            if head -n 30 "${a}" | grep -qs '#.*Makeself'; then
                arch="unpack_makeself";
            fi
        ;;
        *.bin)
            if head -c 100 "${a}" | grep -qs '#.*Makeself'; then
                arch="unpack_makeself";
            fi
        ;;
        *.zip)
            arch="unpack_zip"
        ;;
    esac;
    if [[ ${EAPI} != 7 ]]; then
        case ${m} in 
            *.7z)
                arch="unpack_7z"
            ;;
            *.rar)
                arch="unpack_rar"
            ;;
            *.lha | *.lzh)
                arch="unpack_lha"
            ;;
        esac;
    fi;
    if [[ -z ${arch}${comp} ]]; then
        unpack "$1";
        return $?;
    fi;
    [[ ${arch} != unpack_* ]] && unpack_banner "${a}";
    if [[ -z ${arch} ]]; then
        local _a=${a%.*};
        ${comp} < "${a}" > "${_a##*/}";
    else
        if [[ -z ${comp} ]]; then
            ${arch} "${a}";
        else
            ${comp} < "${a}" | ${arch} -;
        fi;
    fi;
    assert "unpacking ${a} failed (comp=${comp} arch=${arch})"
}
_unpacker_get_decompressor () 
{ 
    case ${1} in 
        *.bz2 | *.tbz | *.tbz2)
            local bzcmd=${PORTAGE_BZIP2_COMMAND:-$(type -P lbzip2 || type -P pbzip2 || type -P bzip2)};
            local bzuncmd=${PORTAGE_BUNZIP2_COMMAND:-${bzcmd} -d};
            : "${UNPACKER_BZ2:=${bzuncmd}}";
            echo "${UNPACKER_BZ2} -c"
        ;;
        *.z | *.gz | *.tgz)
            echo "gzip -dc"
        ;;
        *.lzma | *.xz | *.txz)
            echo "xz -T$(makeopts_jobs) -dc"
        ;;
        *.lz)
            function find_lz_unpacker () 
            { 
                if has_version -b ">=app-arch/xz-utils-5.4.0"; then
                    echo xz;
                    return;
                fi;
                local x;
                for x in plzip pdlzip lzip;
                do
                    type -P ${x} && break;
                done
            };
            : "${UNPACKER_LZIP:=$(find_lz_unpacker)}";
            echo "${UNPACKER_LZIP} -dc"
        ;;
        *.zst)
            echo "zstd -dc"
        ;;
        *.lz4)
            echo "lz4 -dc"
        ;;
        *.lzo)
            echo "lzop -dc"
        ;;
    esac
}
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;
    else
        if [[ $1 =~ "emerge -e @world" ]]; then
            if [[ -n ${pkg-} ]]; then
                echo "%emerge --resume --skipfirst" >> $bl;
            else
                echo "%emerge --resume" >> $bl;
            fi;
        else
            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;
        fi;
    fi
}
declare -fx add2backlog
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' "$@"
}
dist-kernel_PV_to_KV () 
{ 
    debug-print-function ${FUNCNAME} "${@}";
    [[ ${#} -ne 1 ]] && die "${FUNCNAME}: invalid arguments";
    local pv=${1};
    local kv=${pv%%_*};
    [[ -z $(ver_cut 3- "${kv}") ]] && kv+=".0";
    [[ ${pv} == *_* ]] && kv+=-${pv#*_};
    echo "${kv}"
}
dist-kernel_compressed_module_cleanup () 
{ 
    debug-print-function ${FUNCNAME} "${@}";
    [[ ${#} -ne 1 ]] && die "${FUNCNAME}: invalid arguments";
    local path=${1};
    local config_path=/usr/src/linux-${KV_FULL}/.config;
    local option;
    for option in config source/.config build/.config;
    do
        if [[ -f ${path}/${option} ]]; then
            config_path=${path}/${option};
            break;
        fi;
    done;
    local preferred=;
    [[ -f ${config_path} ]] && preferred=$(dist-kernel_get_module_suffix "${config_path}");
    local basename suffix;
    while read -r basename; do
        local prev=;
        for suffix in .ko .ko.gz .ko.xz .ko.zst;
        do
            [[ ${suffix} == ${preferred} ]] && continue;
            local current=${path}/${basename}${suffix};
            [[ -f ${current} ]] || continue;
            if [[ -f ${path}/${basename}${preferred} ]]; then
                rm -v "${current}" || die;
            else
                if [[ -z ${prev} ]]; then
                    prev=${current};
                else
                    if [[ ${current} -nt ${prev} ]]; then
                        rm -v "${prev}" || die;
                        prev=${current};
                    else
                        rm -v "${current}" || die;
                    fi;
                fi;
            fi;
        done;
    done < <(cd "${path}" && find -type f \( -name '*.ko' -o -name '*.ko.gz' -o -name '*.ko.xz' -o -name '*.ko.zst' \) | sed -e 's:[.]ko\(\|[.]gz\|[.]xz\|[.]zst\)$::' | sort | uniq -d || die)
}
dist-kernel_get_image_path () 
{ 
    case ${ARCH} in 
        amd64 | x86)
            echo arch/x86/boot/bzImage
        ;;
        arm64 | riscv)
            if [[ -n ${KERNEL_EFI_ZBOOT} ]]; then
                echo arch/${ARCH}/boot/vmlinuz.efi;
            else
                echo arch/${ARCH}/boot/Image.gz;
            fi
        ;;
        loong)
            if [[ -n ${KERNEL_EFI_ZBOOT} ]]; then
                echo arch/loongarch/boot/vmlinuz.efi;
            else
                echo arch/loongarch/boot/vmlinux.elf;
            fi
        ;;
        arm)
            echo arch/arm/boot/zImage
        ;;
        hppa | ppc | ppc64 | sparc)
            echo ./vmlinux
        ;;
        *)
            die "${FUNCNAME}: unsupported ARCH=${ARCH}"
        ;;
    esac
}
dist-kernel_get_module_suffix () 
{ 
    debug-print-function ${FUNCNAME} "${@}";
    [[ ${#} -eq 1 ]] || die "${FUNCNAME}: invalid arguments";
    local config=${1};
    if ! in_iuse modules-compress || ! use modules-compress; then
        echo .ko;
    else
        if [[ ! -r ${config} ]]; then
            die "Cannot find kernel config ${config}";
        else
            if grep -q "CONFIG_MODULE_COMPRESS_NONE=y" "${config}"; then
                echo .ko;
            else
                if grep -q "CONFIG_MODULE_COMPRESS_GZIP=y" "${config}"; then
                    echo .ko.gz;
                else
                    if grep -q "CONFIG_MODULE_COMPRESS_XZ=y" "${config}"; then
                        echo .ko.xz;
                    else
                        if grep -q "CONFIG_MODULE_COMPRESS_ZSTD=y" "${config}"; then
                            echo .ko.zst;
                        else
                            die "Module compression is enabled, but compressor not known";
                        fi;
                    fi;
                fi;
            fi;
        fi;
    fi
}
dist-kernel_install_kernel () 
{ 
    debug-print-function ${FUNCNAME} "${@}";
    [[ ${#} -eq 3 ]] || die "${FUNCNAME}: invalid arguments";
    local version=${1};
    local image=${2};
    local map=${3};
    local success=;
    while true; do
        nonfatal mount-boot_check_status || break;
        ebegin "Installing the kernel via installkernel";
        ARCH=$(tc-arch-kernel) installkernel "${version}" "${image}" "${map}" || break;
        eend ${?} || die -n "Installing the kernel failed";
        success=1;
        break;
    done;
    if [[ ! -n ${success} ]]; then
        local kernel="<name of your kernel pakcage>:<kernel version>";
        local k_id_file=${image%$(dist-kernel_get_image_path)}/dist-kernel;
        if [[ -f ${k_id_file} ]]; then
            kernel=\'\=$(< ${k_id_file})\';
        fi;
        eerror;
        eerror "The kernel was not deployed successfully. Inspect the failure";
        eerror "in the logs above and once you resolve the problems please";
        eerror "run the equivalent of the following command to try again:";
        eerror;
        eerror "    emerge --config ${kernel}";
        die "Kernel install failed, please fix the problems and run emerge --config";
    fi
}
dist-kernel_reinstall_initramfs () 
{ 
    debug-print-function ${FUNCNAME} "${@}";
    [[ ${#} -eq 2 ]] || die "${FUNCNAME}: invalid arguments";
    local kernel_dir=${1};
    local ver=${2};
    local image_path=${kernel_dir}/$(dist-kernel_get_image_path);
    if [[ ! -f ${image_path} ]]; then
        eerror "Kernel install missing, image not found:";
        eerror "  ${image_path}";
        eerror "Initramfs will not be updated.  Please reinstall your kernel.";
        return;
    fi;
    dist-kernel_install_kernel "${ver}" "${image_path}" "${kernel_dir}/System.map"
}
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 () 
{ 
    local message;
    local log_name;
    while true; do
        case "${1}" in 
            -l | -m)
                [[ $# -lt 2 ]] && die "Must provide an argument to ${1}";
                case "${1}" in 
                    -l)
                        log_name="${2}"
                    ;;
                    -m)
                        message="${2}"
                    ;;
                esac;
                shift 2
            ;;
            *)
                break
            ;;
        esac;
    done;
    [[ -z ${message} ]] && message="Running $@";
    [[ -z ${log_name} ]] && log_name="$(basename ${1})";
    local log_file="${T}/${log_name}.log";
    ebegin "${message}";
    "$@" &> "${log_file}";
    local ret=$?;
    if ! eend $ret; then
        cat "${log_file}";
        die -n "Command \"$@\" failed with exit status $ret";
    fi
}
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 )
}
find_unpackable_file () 
{ 
    local src=$1;
    if [[ -z ${src} ]]; then
        src=${DISTDIR}/${A};
    else
        if [[ ${src} == ./* ]]; then
            :;
        else
            if [[ -e ${DISTDIR}/${src} ]]; then
                src=${DISTDIR}/${src};
            else
                if [[ -e ${PWD}/${src} ]]; then
                    src=${PWD}/${src};
                else
                    if [[ -e ${src} ]]; then
                        src=${src};
                    fi;
                fi;
            fi;
        fi;
    fi;
    [[ ! -e ${src} ]] && return 1;
    echo "${src}"
}
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;
    use prefix && 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_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_makeopts_jobs () 
{ 
    makeopts_jobs "$(_get_all_makeopts)" "${1:-1}"
}
get_makeopts_loadavg () 
{ 
    makeopts_loadavg "$(_get_all_makeopts)" "${1:-999}"
}
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_udevdir () 
{ 
    debug-print-function ${FUNCNAME} "${@}";
    echo "$(_udev_get_udevdir)"
}
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 <VARIABLE> <CONFIGFILE>";
    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= -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 <VARIABLE> <CONFIGFILE>";
    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 <USEFLAG>" 1>&2;
        die "in_iuse() called without a parameter";
    fi;
    local liuse=(${IUSE_EFFECTIVE});
    has "${use}" "${liuse[@]#[+-]}"
}
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 [[ ${MERGE_TYPE} == binary && -z ${SKIP_KERNEL_BINPKG_ENV_RESET} ]]; then
        unset KV_FULL _LINUX_CONFIG_EXISTS_DONE KV_OUT_DIR;
        SKIP_KERNEL_BINPKG_ENV_RESET=1;
    fi;
    if ! get_version; then
        ewarn "Unable to calculate Linux Kernel version for build, attempting to use running version";
    fi;
    if [[ -z ${KV_FULL} ]] && ! get_running_version; then
        die "Unable to determine any Linux Kernel version, please report a bug";
    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;
    dist-kernel_compressed_module_cleanup "${EROOT}/lib/modules/${KV_FULL}";
    _modules_update_depmod;
    if [[ -z ${ROOT} && -n ${MODULES_INITRAMFS_IUSE} ]] && use dist-kernel && use ${MODULES_INITRAMFS_IUSE#+}; then
        dist-kernel_reinstall_initramfs "${KV_DIR}" "${KV_FULL}";
    fi;
    if has_version virtual/dist-kernel && ! use dist-kernel; then
        ewarn "virtual/dist-kernel is installed, but USE=\"dist-kernel\"";
        ewarn "is not enabled for ${CATEGORY}/${PN}.";
        ewarn "It's recommended to globally enable the dist-kernel USE flag";
        ewarn "to automatically trigger initramfs rebuilds on kernel updates";
    fi;
    [[ -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]} "${@}";
    _MODULES_GLOBAL[ran:pkg_setup]=1;
    _modules_check_function ${#} 0 0 || return 0;
    if [[ -z ${ROOT} && -n ${MODULES_INITRAMFS_IUSE} ]] && use dist-kernel && use ${MODULES_INITRAMFS_IUSE#+}; then
        nonfatal mount-boot_check_status;
    fi;
    [[ ${MERGE_TYPE} != binary ]] || 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 '' "<module>..." || return 0;
    ( insinto "/lib/modules/${KV_FULL}/${_MODULES_GLOBAL[moduleinto]:-extra}";
    doins "${@}" )
}
linux_moduleinto () 
{ 
    debug-print-function ${FUNCNAME[0]} "${@}";
    _modules_check_function ${#} 1 1 "<install-dir>" || return 0;
    _MODULES_GLOBAL[moduleinto]=${1}
}
makeopts_jobs () 
{ 
    [[ $# -eq 0 ]] && set -- "$(_get_all_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 -- "$(_get_all_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 '[<path>]' || 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_dracut.conf.d "${mods[@]##*/}";
    _modules_process_strip "${mods[@]}";
    _modules_process_sign "${mods[@]}";
    _modules_sanity_modversion "${mods[@]}";
    _modules_process_compress "${mods[@]}";
    _MODULES_GLOBAL[ran:post_process]=1
}
mount-boot_check_status () 
{ 
    mount-boot_is_disabled && return 0;
    local partition=;
    local part_is_not_mounted=;
    local part_is_read_only=;
    local candidates=(/boot);
    if [[ -d /sys/firmware/efi ]]; then
        candidates+=(/efi /boot/efi /boot/EFI);
    fi;
    for partition in ${candidates[@]};
    do
        local fstabstate=$(awk "!/^[[:blank:]]*#|^\/dev\/BOOT/ && \$2 == \"${partition}\" 			{ print 1; exit }" /etc/fstab || die "awk failed");
        if [[ -z ${fstabstate} ]]; then
            einfo "Assuming you do not have a separate ${partition} partition.";
        else
            local procstate=$(awk "\$2 == \"${partition}\" { split(\$4, a, \",\"); 				for (i in a) if (a[i] ~ /^r[ow]\$/) { print a[i]; break }; exit }" /proc/mounts || die "awk failed");
            if [[ -z ${procstate} ]]; then
                eerror "Your ${partition} partition is not mounted";
                eerror "Please mount it and retry.";
                die -n "${partition} not mounted";
                part_is_not_mounted=1;
            else
                if [[ ${procstate} == ro ]]; then
                    eerror "Your ${partition} partition, was detected as being mounted," "but is mounted read-only.";
                    eerror "Please remount it as read-write and retry.";
                    die -n "${partition} mounted read-only";
                    part_is_read_only=1;
                else
                    einfo "Your ${partition} partition was detected as being mounted.";
                    einfo "Files will be installed there for ${PN} to function correctly.";
                fi;
            fi;
        fi;
    done;
    if [[ -n ${part_is_not_mounted} ]]; then
        return 1;
    else
        if [[ -n ${part_is_read_only} ]]; then
            return 2;
        else
            return 0;
        fi;
    fi
}
mount-boot_is_disabled () 
{ 
    if [[ -n ${EROOT} ]]; then
        return 0;
    fi;
    if [[ ${MERGE_TYPE} == buildonly ]]; then
        return 0;
    fi;
    if [[ -n ${DONT_MOUNT_BOOT} ]]; then
        return 0;
    fi;
    return 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
}
number_abis () 
{ 
    set -- `get_install_abis`;
    echo $#
}
pkg_nofetch () 
{ 
    default
}
pkg_postinst () 
{ 
    if use udev; then
        udev_reload;
    fi;
    linux-mod-r1_pkg_postinst
}
pkg_postrm () 
{ 
    if use udev; then
        udev_reload;
    fi
}
pkg_setup () 
{ 
    linux-mod-r1_pkg_setup "$@"
}
post_src_install () 
{ 
    if [[ ${PORTAGE_USE_CLANG_HOOK} == 1 && -f "${EROOT}"/var/tmp/clang/${CATEGORY}/${PF}/clang16-broken ]]; then
        if grep -q "error:.*C99" "${EROOT}"/var/tmp/clang/${CATEGORY}/${PF}/clang.diff; then
            eqawarn "Clang 16 testing: Found possible issues in configure!";
            eqawarn "Clang 16 testing: Please check "${EROOT}"/var/tmp/clang/${CATEGORY}/${PF}/clang.diff";
        fi;
    fi;
    __tinderbox_meson
}
pre_src_compile () 
{ 
    if [[ -f "${T}"/clang16-errors.log ]]; then
        rm -rf "${EROOT}"/var/tmp/clang/${CATEGORY}/${PF};
        mkdir -p "${EROOT}"/var/tmp/clang/${CATEGORY}/${PF};
        cp -rv "${T}"/clang16-{errors,safe}.log "${EROOT}"/var/tmp/clang/${CATEGORY}/${PF};
        if diff -ruN "${T}"/clang16-{safe,errors}.log > "${EROOT}"/var/tmp/clang/${CATEGORY}/${PF}/clang.diff; then
            rm "${EROOT}"/var/tmp/clang/${CATEGORY}/${PF}/clang.diff;
        fi;
        [[ -f "${T}"/clang16-broken ]] && touch "${EROOT}"/var/tmp/clang/${CATEGORY}/${PF}/clang16-broken;
    fi;
    export PORTAGE_CLANG_HOOK_USE_REAL_COMPILER=1
}
pre_src_configure () 
{ 
    if [[ ${PORTAGE_USE_CLANG_HOOK} == 1 ]]; then
        if [[ -n ${CC} && ${CC} != *clang* && -z ${PORTAGE_USE_CLANG_HOOK_GCC} ]]; then
            return;
        fi;
        if ! type -P ansifilter &> /dev/null; then
            return;
        fi;
        ewarn "Modern C testing: this build is using a /etc/portage/bashrc hook ($hook_timestamp)!";
        ewarn "Modern C testing: see https://wiki.gentoo.org/wiki/Modern_C_porting for more info.";
        export ac_cv_c_undeclared_builtin_options="none needed";
        export gl_cv_compiler_check_decl_option="-Werror=implicit-function-declaration";
        if [[ ${CHOST} == *musl* ]]; then
            if has_version dev-libs/libbsd; then
                export ac_cv_func___fpurge=yes;
                export ac_cv_func_fpurge=yes;
                export ac_cv_have_decl_fpurge=no;
                export gl_cv_func_fpurge_works=no;
            fi;
            export ac_cv_header_sys_types_h_makedev=no;
            export gl_cv_minmax_in_limits_h=no;
        else
            export ac_cv_have_decl_strerror_r="yes";
        fi;
        has waf-utils ${INHERITED} && return;
        has qmake-utils ${INHERITED} && return;
        has qt5-build ${INHERITED} && return;
        if grep -q "x11-misc/imake" <<< "${BDEPEND}"; then
            return;
        fi;
        __PORTAGE_HOOK_CLANG=$(type -P "${__PORTAGE_HOOK_CLANG}");
        mkdir "${T}"/clang-wrappers;
        cat <<-EOF > "${T}"/clang-wrappers/clang
#!/usr/bin/env bash
hook_clang=${__PORTAGE_HOOK_CLANG}
real_compiler=${__PORTAGE_HOOK_CLANG}

if [[ -n \${PORTAGE_USE_CLANG_HOOK_GCC} ]] ; then
if [[ -n \${CC} && \${CC##*/} == *clang* ]] ; then
:;
else
real_compiler="${BROOT:-/}"/usr/bin/${CHOST}-gcc
fi
fi

if [[ \$0 == *++ ]]; then
real_compiler=\${real_compiler/clang/clang++}
real_compiler=\${real_compiler/gcc/g++}
hook_clang=\${hook_clang/clang/clang++}
hook_clang=\${hook_clang/gcc/g++}
fi

if [[ \${PORTAGE_CLANG_HOOK_USE_REAL_COMPILER} -gt 1 ]]; then
# clang's self recursing... try your best!
case "\${real_compiler}" in
*++*) real_compiler="/usr/bin/\${CHOST+\${CHOST}-}g++" ;;
*) real_compiler="/usr/bin/\${CHOST+\${CHOST}-}gcc" ;;
esac
real_compiler="\${real_compiler/clang/gcc}"
fi

# Safety net against recursive calls
PORTAGE_orig_USE_REAL_COMP="\${PORTAGE_CLANG_HOOK_USE_REAL_COMPILER}"
export PORTAGE_CLANG_HOOK_USE_REAL_COMPILER=\$((PORTAGE_CLANG_HOOK_USE_REAL_COMPILER+1))

if [[ \${PORTAGE_orig_USE_REAL_COMP} ]]; then
exec \${real_compiler} "\$@"
fi

export CFLAGS="${CFLAGS/-fdiagnostics-color=always}"
export CFLAGS="${CFLAGS/-fdiagnostics-urls=never}"

# - Need > /dev/null for sys-libs/musl
# - No LTO because of the noise it generates in diffs (temps)
cl1() {
\${hook_clang} -fno-lto -Wno-unused-command-line-argument 				-Wno-error=implicit-function-declaration 				-Wno-error=implicit-int 				-Wno-error=int-conversion 				-Wno-error=incompatible-function-pointer-types 				-Wno-error=incompatible-pointer-types 				-Wno-error=return-type 				${CFLAGS} 				\$@ 2>&1                                 -fdiagnostics-color=never | ansifilter | sed 				-e "s:14.0.6:14.ignoreme:g" 				-e "s:15.0.0:14.ignoreme:g" 				-e "s:clang-\(14\|15\|16\|17\|18\):clang-ignoreme:g" 				-e 's:clang version \([0-9]\+\)\.[0-9]\.[0-9]:clang version ignoreme:' 				-e "s:/usr/lib/llvm/\(14\|15\|16\|17\|18\)/:/usr/lib/llvm/ignoreme/:g" 				-e "s:conftest-.*\.o:conftest.o:g" 				-e "s_conftest\.c\:[0-9]\+\:[0-9]\+_ignoreme_g" 				-e "s:garbage2:ignoreme:" 				-e "s:garbage:ignoreme:" 				-e "/ac_nonexistent.h/d" 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: no input files/d' 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: unsupported option/d' 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: unknown argument/d' 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: no such file or directory/d' 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: linker command failed/d' 				-e '/[0-9]\+ \(warning\|error\) generated/d' | tee -a "${T}"/clang16-safe.log > /dev/null

if ! [[ \${PIPESTATUS[0]} -eq 0 ]] ; then
touch "${T}"/clang16-safe-failed
fi
}
# TODO: No -Werror=strict-prototypes here for now as AC_PROG_LEX, AC_CHECK_FUNCS rely on it
# also, I think Clang 15.0.1 (which reverts the other bits) keeps that in anyway.
cl2() {
\${hook_clang} -fno-lto -Wno-unused-command-line-argument 				-Werror=implicit-function-declaration 				-Werror=implicit-int 				-Werror=int-conversion 				-Werror=incompatible-function-pointer-types 				-Werror=incompatible-pointer-types 				-Werror=return-type 				${CFLAGS} 				\$@ 2>&1 				-fdiagnostics-color=never | ansifilter | sed 				-e "s:14.0.6:14.ignoreme:g" 				-e "s:15.0.0:14.ignoreme:g" 				-e "s:clang-\(14\|15\|16\|17\|18\):clang-ignoreme:g" 				-e 's:clang version \([0-9]\+\)\.[0-9]\.[0-9]:clang version ignoreme:' 				-e "s:/usr/lib/llvm/\(14\|15\|16\|17\|18\)/:/usr/lib/llvm/ignoreme/:g" 				-e "s:15:14:g" 				-e "s:conftest-.*\.o:conftest.o:g" 				-e "s_conftest\.c\:[0-9]\+\:[0-9]\+_ignoreme_g" 				-e "s:garbage2:ignoreme:" 				-e "s:garbage:ignoreme:" 				-e "/ac_nonexistent.h/d" 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: no input files/d' 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: unsupported option/d' 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: unknown argument/d' 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: no such file or directory/d' 				-e '/clang-\(14\|15\|16\|17\|18\|ignoreme\): error: linker command failed/d' 				-e '/[0-9]\+ \(warning\|error\) generated/d' | tee -a "${T}"/clang16-errors.log > /dev/null

if ! [[ \${PIPESTATUS[0]} -eq 0 ]] ; then
touch "${T}"/clang16-errors-failed
fi
}

# Safety net against recursive calls
export PORTAGE_CLANG_HOOK_USE_REAL_COMPILER=1
# Because clang can invoke GCC
export PORTAGE_USE_CLANG_HOOK_GCC=1

# - Just run it again as it's easier for anything which wants to parse stdout/stderr,
# and we're not concerned about performance for this experiment anyway.
# - We have to do the tee & pipe dance to not greedily consume stdin: bug 870985.
# - Timeout as a safety net because we don't ever want to make a build hang. Occurs
# with waf sometimes (being investigated), but we should keep the timeout after that anyway.
timeout --preserve-status -s PIPE 10 tee -p >(cl1 "\$@" -o "${T}"/garbage.\$\$) >(cl2 "\$@" -o "${T}"/garbage2.\$\$) | \${real_compiler} "\$@"
ret="\${PIPESTATUS[1]}"

# If at least one of them succeeded, then complain if *only* one of them did.
if [[ -f "${T}"/clang16-safe-failed || -f "${T}"/clang16-errors-failed ]] ; then
if ! [[ -f "${T}"/clang16-safe-failed && -f "${T}"/clang16-errors-failed ]] ; then
touch "${T}"/clang16-broken
fi
fi

rm -f "${T}"/clang16-safe-failed "${T}"/clang16-errors-failed
exit \${ret}
EOF

        chmod +x "${T}"/clang-wrappers/clang;
        if in_iuse clang; then
            :;
        else
            for alias in ${CHOST}-gcc gcc ${CHOST}-clang ${CHOST}-g++ g++ ${CHOST}-clang++;
            do
                ln -s "${T}"/clang-wrappers/clang "${T}"/clang-wrappers/${alias} || exit 1;
                chmod +x "${T}"/clang-wrappers/${alias};
            done;
            export CFLAGS="${CFLAGS} -Werror=implicit-function-declaration -Werror=implicit-int";
            export PATH="${T}/clang-wrappers:${PATH}";
        fi;
    fi
}
pre_src_prepare () 
{ 
    if [[ -n ${CC} && ${CC} != *clang* ]]; then
        return;
    fi;
    case ${EAPI} in 
        [0123456])
            hv_args="--host-root"
        ;;
        *)
            hv_args="-b"
        ;;
    esac;
    local ver;
    for ver in 15 16 17 18;
    do
        has_version ${hv_args} sys-devel/clang:${ver} && __PORTAGE_HOOK_CLANG=clang-${ver};
    done;
    __PORTAGE_HOOK_CLANG=$(type -P "${__PORTAGE_HOOK_CLANG}");
    if ! type -P ansifilter &> /dev/null; then
        return;
    fi;
    if [[ -z ${__PORTAGE_HOOK_CLANG} ]] || ! type -P ${__PORTAGE_HOOK_CLANG} &> /dev/null; then
        export CC=gcc;
        export CXX=g++;
        return;
    fi
}
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}"
}
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)
}
source_profile () 
{ 
    set +u;
    source /etc/profile;
    set -u
}
declare -fx source_profile
src_compile () 
{ 
    MODULES_MAKEARGS+=(KDIR="${KV_OUT_DIR}");
    emake "${MODULES_MAKEARGS[@]}"
}
src_configure () 
{ 
    default
}
src_install () 
{ 
    linux_moduleinto kernel/drivers/net/wireless/${PN};
    linux_domodule aic8800_fdrv/aic8800_fdrv.ko aic_load_fw/aic_load_fw.ko;
    modules_post_process;
    if use firmware; then
        insinto /lib/firmware;
        doins -r "${WORKDIR}/lib/firmware/aic8800DC";
    fi;
    if use udev; then
        udev_newrules "${WORKDIR}/lib/udev/rules.d/aic.rules" 99-aic-modeswitch.rules;
    fi
}
src_prepare () 
{ 
    default
}
src_test () 
{ 
    default
}
src_unpack () 
{ 
    unpacker_src_unpack "$@"
}
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;
        else
            if ! emaint merges --fix &>> $synclog; then
                ReachedEOL "broken repo, cannot be fixed" $synclog;
            else
                if ! emaint sync --auto &>> $synclog; then
                    ReachedEOL "broken sync of repo" $synclog;
                fi;
            fi;
        fi;
    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 + 2 * 3600)) second ago }..@{ 2 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 | arm64-apple-darwin*)
            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) || defined(_LIBCPP_ENABLE_HARDENED_MODE)" ${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
        ;;
        arc*b*)
            echo big
        ;;
        arc*)
            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-build-ptr-size () 
{ 
    $(tc-getBUILD_CPP) -P - <<< __SIZEOF_POINTER__ || die "Could not determine CBUILD pointer size"
}
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 <ciso646>

#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-get-ptr-size () 
{ 
    $(tc-getCPP) -P - <<< __SIZEOF_POINTER__ || die "Could not determine CHOST pointer size"
}
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-64bit-time_t () 
{ 
    $(tc-getCC) ${CFLAGS} ${CPPFLAGS} -c -x c - -o /dev/null <<-EOF &> /dev/null
#include <sys/types.h>
int test[sizeof(time_t) >= 8 ? 1 : -1];
EOF

    return $?
}
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;
    case "${CHOST}" in 
        *-darwin*)
            : ${flags:=-dynamiclib}
        ;;
        *)
            : ${flags:=-fPIC -shared -Wl,-z,defs}
        ;;
    esac;
    [[ $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-lto () 
{ 
    local f="${T}/test-lto.o";
    local ret=1;
    case $(tc-get-compiler-type) in 
        clang)
            $(tc-getCC) ${CFLAGS} -c -o "${f}" -x c - <<< "" || die;
            llvm-bcanalyzer "${f}" &> /dev/null && ret=0
        ;;
        gcc)
            $(tc-getCC) ${CFLAGS} -c -o "${f}" -x c - <<< "" || die;
            [[ $($(tc-getREADELF) -S "${f}") == *.gnu.lto* ]] && ret=0
        ;;
    esac;
    rm -f "${f}" || die;
    return "${ret}"
}
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-bfd "$@"; then
        return;
    fi;
    ewarn "Forcing usage of the BFD linker";
    local ld=$(unset 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 CFLAGS="${CFLAGS} -fuse-ld=bfd";
        export CXXFLAGS="${CXXFLAGS} -fuse-ld=bfd";
        export LDFLAGS="${LDFLAGS} -fuse-ld=bfd";
    fi
}
tc-ld-is-bfd () 
{ 
    local out;
    local -x LC_ALL=C;
    out=$($(tc-getLD "$@") --version 2>&1);
    if [[ ${out} != "GNU ld"* ]]; then
        return 1;
    fi;
    local base="${T}/test-tc-linker";
    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 ld".* ]]; then
        return 1;
    fi;
    return 0
}
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-linker";
    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-linker";
    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-ld-is-mold () 
{ 
    local out;
    local -x LC_ALL=C;
    out=$($(tc-getLD "$@") --version 2>&1);
    if [[ ${out} == *"mold"* ]]; then
        return 0;
    fi;
    local base="${T}/test-tc-linker";
    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} == *"mold"* ]]; 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 
        arm64*)
            echo arm64
        ;;
        aarch64*)
            echo arm64
        ;;
        alpha*)
            echo alpha
        ;;
        arc*)
            echo arc
        ;;
        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"
        ;;
        arm64-apple-darwin*)
            echo "no"
        ;;
        arm*)
            echo "yes"
        ;;
        *)
            echo "no"
        ;;
    esac
}
udev_dorules () 
{ 
    debug-print-function ${FUNCNAME} "${@}";
    ( insopts -m 0644;
    insinto "$(_udev_get_udevdir)"/rules.d;
    doins "${@}" )
}
udev_get_udevdir () 
{ 
    debug-print-function ${FUNCNAME} "${@}";
    eerror "This ebuild should be using the get_udevdir() function instead of the deprecated udev_get_udevdir()";
    die "Deprecated function call: udev_get_udevdir(), please report to (overlay) maintainers."
}
udev_newrules () 
{ 
    debug-print-function ${FUNCNAME} "${@}";
    ( insopts -m 0644;
    insinto "$(_udev_get_udevdir)"/rules.d;
    newins "${@}" )
}
udev_reload () 
{ 
    if [[ -n ${ROOT%/} ]]; then
        return 0;
    fi;
    if [[ -d ${ROOT}/run/udev ]]; then
        ebegin "Running udev control --reload for reloading rules and databases";
        udevadm control --reload;
        eend $?;
    fi
}
unpack_7z () 
{ 
    [[ $# -eq 1 ]] || die "Usage: ${FUNCNAME} <file>";
    local p7z=$(find_unpackable_file "$1");
    unpack_banner "${p7z}";
    local output;
    output="$(7z x -y "${p7z}")";
    if [ $? -ne 0 ]; then
        echo "${output}" 1>&2;
        die "unpacking ${p7z} failed (arch=unpack_7z)";
    fi
}
unpack_banner () 
{ 
    echo ">>> Unpacking ${1##*/} to ${PWD}"
}
unpack_cpio () 
{ 
    [[ $# -eq 1 ]] || die "Usage: ${FUNCNAME} <file>";
    local cpio_cmd=(cpio --make-directories --extract --preserve-modification-time);
    if [[ $1 == "-" ]]; then
        unpack_banner "stdin";
        "${cpio_cmd[@]}";
    else
        local cpio=$(find_unpackable_file "$1");
        unpack_banner "${cpio}";
        "${cpio_cmd[@]}" < "${cpio}";
    fi
}
unpack_deb () 
{ 
    [[ $# -eq 1 ]] || die "Usage: ${FUNCNAME} <file>";
    local deb=$(find_unpackable_file "$1");
    unpack_banner "${deb}";
    { 
        if [[ -n ${EPREFIX} ]]; then
            { 
                read;
                [[ ${REPLY} = "!<arch>" ]] || die "${deb} does not seem to be a deb archive";
                local f timestamp uid gid mode size magic;
                while read f timestamp uid gid mode size magic; do
                    [[ -n ${f} && -n ${size} ]] || continue;
                    f=${f%/};
                    if [[ ${f} = "data.tar"* ]]; then
                        local decomp=$(_unpacker_get_decompressor "${f}");
                        head -c "${size}" | ${decomp:-cat};
                        assert "unpacking ${f} from ${deb} failed";
                        break;
                    else
                        head -c "${size}" > /dev/null;
                    fi;
                done
            } < "${deb}";
        else
            local f=$($(tc-getBUILD_AR) t "${deb}" | grep ^data.tar
assert "data not found in ${deb}");
            local decomp=$(_unpacker_get_decompressor "${f}");
            $(tc-getBUILD_AR) p "${deb}" "${f}" | ${decomp:-cat};
            assert "unpacking ${f} from ${deb} failed";
        fi
    } | tar --no-same-owner -xf -;
    assert "unpacking ${deb} failed"
}
unpack_gpkg () 
{ 
    [[ $# -eq 1 ]] || die "Usage: ${FUNCNAME} <file>";
    local gpkg=$(find_unpackable_file "$1");
    unpack_banner "${gpkg}";
    local l images=();
    while read -r l; do
        case ${l} in 
            */image.tar*.sig)

            ;;
            */image.tar*)
                images+=("${l}")
            ;;
        esac;
    done < <(tar -tf "${gpkg}" || die "unable to list ${gpkg}");
    if [[ ${#images[@]} -eq 0 ]]; then
        die "No image.tar found in ${gpkg}";
    else
        if [[ ${#images[@]} -gt 1 ]]; then
            die "More than one image.tar found in ${gpkg}";
        fi;
    fi;
    local decomp=$(_unpacker_get_decompressor "${images[0]}");
    local dirname=${images[0]%/*};
    mkdir -p "${dirname}" || die;
    tar -xOf "${gpkg}" "${images[0]}" | ${decomp:-cat} | tar --no-same-owner -C "${dirname}" -xf -;
    assert "Unpacking ${gpkg} failed"
}
unpack_lha () 
{ 
    [[ $# -eq 1 ]] || die "Usage: ${FUNCNAME} <file>";
    local lha=$(find_unpackable_file "$1");
    unpack_banner "${lha}";
    lha xfq "${lha}" || die "unpacking ${lha} failed (arch=unpack_lha)"
}
unpack_makeself () 
{ 
    local src_input=${1:-${A}};
    local src=$(find_unpackable_file "${src_input}");
    local skip=$2;
    local exe=$3;
    [[ -z ${src} ]] && die "Could not locate source for '${src_input}'";
    unpack_banner "${src}";
    if [[ -z ${skip} ]]; then
        local ver=$(grep -m1 -a '#.*Makeself' "${src}" | awk '{print $NF}');
        local skip=0;
        exe=tail;
        case ${ver} in 
            1.5.* | 1.6.0-nv*)
                skip=$(grep -a ^skip= "${src}" | cut -d= -f2)
            ;;
            2.0 | 2.0.1)
                skip=$(grep -a ^'	'tail "${src}" | awk '{print $2}' | cut -b2-)
            ;;
            2.1.1)
                skip=$(grep -a ^offset= "${src}" | awk '{print $2}' | cut -b2-);
                (( skip++ ))
            ;;
            2.1.2)
                skip=$(grep -a ^offset= "${src}" | awk '{print $3}' | head -n 1);
                (( skip++ ))
            ;;
            2.1.3)
                skip=`grep -a ^offset= "${src}" | awk '{print $3}'`;
                (( skip++ ))
            ;;
            2.1.4 | 2.1.5 | 2.1.6 | 2.2.0 | 2.3.0 | 2.4.0)
                skip=$(grep -a offset=.*head.*wc "${src}" | awk '{print $3}' | head -n 1);
                skip=$(head -n ${skip} "${src}" | wc -c);
                exe="dd"
            ;;
            2.4.5)
                skip=$(sed -n -e '/^skip=/{s:skip="\(.*\)":\1:p;q}' "${src}");
                skip=$(head -n "${skip}" "${src}" | wc -c);
                exe="dd"
            ;;
            *)
                eerror "I'm sorry, but I was unable to support the Makeself file.";
                eerror "The version I detected was '${ver}'.";
                eerror "Please file a bug about the file ${src##*/} at";
                eerror "https://bugs.gentoo.org/ so that support can be added.";
                die "makeself version '${ver}' not supported"
            ;;
        esac;
        debug-print "Detected Makeself version ${ver} ... using ${skip} as offset";
    fi;
    case ${exe} in 
        tail)
            exe=(tail -n +${skip} "${src}")
        ;;
        dd)
            exe=(dd ibs=${skip} skip=1 if="${src}")
        ;;
        *)
            die "makeself can't handle exe '${exe}'"
        ;;
    esac;
    local decomp= filetype suffix;
    filetype=$("${exe[@]}" 2> /dev/null | head -c 512 | file -S -b -) || die;
    case ${filetype} in 
        *tar\ archive*)
            decomp=cat
        ;;
        bzip2*)
            suffix=bz2
        ;;
        gzip*)
            suffix=gz
        ;;
        compress*)
            suffix=z
        ;;
        XZ*)
            suffix=xz
        ;;
        Zstandard*)
            suffix=zst
        ;;
        lzop*)
            suffix=lzo
        ;;
        LZ4*)
            suffix=lz4
        ;;
        "ASCII text"*)
            decomp='base64 -d'
        ;;
        *)
            die "Unknown filetype \"${filetype}\", for makeself ${src##*/} ('${ver}' +${skip})"
        ;;
    esac;
    [[ -z ${decomp} ]] && decomp=$(_unpacker_get_decompressor ".${suffix}");
    "${exe[@]}" | ${decomp} | tar --no-same-owner -xf -;
    assert "failure unpacking (${filetype}) makeself ${src##*/} ('${ver}' +${skip})"
}
unpack_pdv () 
{ 
    local src=$(find_unpackable_file "$1");
    local sizeoff_t=$2;
    [[ -z ${src} ]] && die "Could not locate source for '$1'";
    [[ -z ${sizeoff_t} ]] && die "No idea what off_t size was used for this pdv :(";
    unpack_banner "${src}";
    local metaskip=$(tail -c ${sizeoff_t} "${src}" | hexdump -e \"%i\");
    local tailskip=$(tail -c $((${sizeoff_t}*2)) "${src}" | head -c ${sizeoff_t} | hexdump -e \"%i\");
    local metafile="${T}/${FUNCNAME}.meta";
    tail -c +$((${metaskip}+1)) "${src}" > "${metafile}";
    local datafile=$(tail -c +$((${metaskip}+1)) "${src}" | strings | head -n 1);
    datafile=$(basename "${datafile}");
    local tmpfile="${T}/${FUNCNAME}";
    tail -c +$((${tailskip}+1)) ${src} 2> /dev/null | head -c 512 > "${tmpfile}";
    local iscompressed=$(file -S -b "${tmpfile}");
    if [[ ${iscompressed:0:8} == "compress" ]]; then
        iscompressed=1;
        mv "${tmpfile}"{,.Z};
        gunzip "${tmpfile}";
    else
        iscompressed=0;
    fi;
    local istar=$(file -S -b "${tmpfile}");
    if [[ ${istar:0:9} == "POSIX tar" ]]; then
        istar=1;
    else
        istar=0;
    fi;
    if [ ${iscompressed} -eq 1 ]; then
        if [ ${istar} -eq 1 ]; then
            tail -c +$((${tailskip}+1)) "${src}" 2> /dev/null | head -c $((${metaskip}-${tailskip})) | tar -xzf -;
        else
            tail -c +$((${tailskip}+1)) "${src}" 2> /dev/null | head -c $((${metaskip}-${tailskip})) | gzip -dc > ${datafile};
        fi;
    else
        if [ ${istar} -eq 1 ]; then
            tail -c +$((${tailskip}+1)) "${src}" 2> /dev/null | head -c $((${metaskip}-${tailskip})) | tar --no-same-owner -xf -;
        else
            tail -c +$((${tailskip}+1)) "${src}" 2> /dev/null | head -c $((${metaskip}-${tailskip})) > ${datafile};
        fi;
    fi;
    true
}
unpack_rar () 
{ 
    [[ $# -eq 1 ]] || die "Usage: ${FUNCNAME} <file>";
    local rar=$(find_unpackable_file "$1");
    unpack_banner "${rar}";
    unrar x -idq -o+ "${rar}" || die "unpacking ${rar} failed (arch=unpack_rar)"
}
unpack_zip () 
{ 
    [[ $# -eq 1 ]] || die "Usage: ${FUNCNAME} <file>";
    local zip=$(find_unpackable_file "$1");
    unpack_banner "${zip}";
    unzip -qo "${zip}";
    [[ $? -le 1 ]] || die "unpacking ${zip} failed (arch=unpack_zip)"
}
unpacker () 
{ 
    local a;
    [[ $# -eq 0 ]] && set -- ${A};
    for a in "$@";
    do
        _unpacker "${a}";
    done
}
unpacker_src_unpack () 
{ 
    unpacker
}
unpacker_src_uri_depends () 
{ 
    local uri;
    local -A deps;
    if [[ $# -eq 0 ]]; then
        set -f;
        set -- ${SRC_URI};
        set +f;
    fi;
    for uri in "$@";
    do
        case ${uri,,} in 
            *.cpio.* | *.cpio)
                deps[cpio]="app-alternatives/cpio"
            ;;
            *.rar)
                deps[rar]="app-arch/unrar"
            ;;
            *.7z)
                deps[7z]="app-arch/p7zip"
            ;;
            *.xz)
                deps[xz]="app-arch/xz-utils"
            ;;
            *.zip)
                deps[zip]="app-arch/unzip"
            ;;
            *.lz)
                deps[lz]="
				|| (
					>=app-arch/xz-utils-5.4.0
					app-arch/plzip
					app-arch/pdlzip
					app-arch/lzip
				)
			"
            ;;
            *.zst)
                deps[zst]="app-arch/zstd"
            ;;
            *.lha | *.lzh)
                deps[lhah]="app-arch/lha"
            ;;
            *.lz4)
                deps[lz4]="app-arch/lz4"
            ;;
            *.lzo)
                deps[lzo]="app-arch/lzop"
            ;;
        esac;
    done;
    echo "${deps[*]}"
}
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
}