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