freebsd-skq/sys/modules
jhibbits 476a473cab powerpc64/powernv: Add opal NVRAM driver for PowerNV systems
Add a very basic NVRAM driver for OPAL which can be used by the IBM
powerpc-utils nvram utility, not to be confused with the base nvram utility,
which only operates on powermac_nvram.

The IBM utility handles all partitions itself, treating the nvram device as
a plain store.

An alternative would be to manage partitions in the kernel, and augment the
base nvram utility to deal with different backing stores, but that
complicates the driver significantly.  Instead, present the same interface
IBM's utlity expects, and we get the usage for free.

Tested by:	bdragon
2019-09-14 03:30:34 +00:00
..
3dfx
3dfx_linux
aac Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
aacraid Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
accf_data
accf_dns
accf_http
acl_nfs4
acl_posix1e
acpi
adlink Convert the PCI ID selection from a simple if into a table. 2018-03-23 15:35:19 +00:00
ae
aesni Add an AESNI-optimized version of the CCM/CBC cryptographic and authentication 2019-05-25 07:26:30 +00:00
age
agp
ahci
aic7xxx META_MODE: Fix wanting a meta file in source tree. 2018-07-04 00:18:40 +00:00
alc
ale
allwinner The pwm interface was replaced with pwmbus, include the right header file. 2019-06-16 00:27:11 +00:00
alq
am335x_dmtpps
amd_ecc_inject
amdgpio Add amdgpio, driver for GPIO controller on AMD-based x86_64 platforms 2018-10-21 04:52:37 +00:00
amdsbwd Add missing generated header file. 2018-07-09 14:18:03 +00:00
amdsmb Update AMDSMB to use PCI_MATCH 2018-07-07 15:55:52 +00:00
amdsmn
amdtemp
amr
an
aout
apm
ar71xx
arcmsr
arm_ti Add module makefiles for Texas Instruments ARM SoCs. 2019-06-16 01:22:44 +00:00
armv8crypto Create an empty stdint.h for arm_neon.h to include. 2018-07-16 15:39:33 +00:00
asmc Yank crufty INTR_FILTER option 2018-05-24 17:06:00 +00:00
ata
ath
ath_ahb
ath_dfs
ath_hal
ath_hal_ar5210
ath_hal_ar5211
ath_hal_ar5212
ath_hal_ar5416 Garbage collect AH_SUPPORT_AR5416 config option. 2019-01-25 13:48:40 +00:00
ath_hal_ar9300
ath_main
ath_pci
ath_rate
autofs
auxio
bce
bcm283x_clkman Forgot to add the skeleton BCM283x Clock Manager 2018-01-22 08:33:59 +00:00
bcm283x_pwm
bfe
bge
bhnd
bios Retire CLANG_NO_IAS34 2018-11-01 23:11:47 +00:00
bktr
blake2 Silence non-actionable warnings in vendor code 2018-05-19 00:04:01 +00:00
bnxt
bridgestp
bwi
bwn bwn(4): Fix outstanding bug in PHY-G tssi2dbm table generation caught by 2018-02-12 22:21:11 +00:00
bxe disable set but not used on code that can't be changed 2018-05-19 04:46:34 +00:00
bytgpio
cam Add nvme_util.c to cam.ko. 2018-04-07 19:29:19 +00:00
cardbus
carp
cas
cbb
cc
ccp
cd9660
cd9660_iconv
ce
cfi Remove kernel support for armeb 2018-07-17 23:23:45 +00:00
cfiscsi
chromebook_platform
chvgpio [chvgpio] add GPIO driver for Intel Z8xxx SoC family 2018-02-22 19:12:32 +00:00
ciss
cloudabi
cloudabi32
cloudabi64
cmx
coretemp
cp
cpsw
cpuctl
cpufreq
crypto Expose zlib's utility functions in Z_SOLO library when building kernel. 2019-08-07 01:41:17 +00:00
cryptodev Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
ctau
ctl
cuse Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
cx
cxgb
cxgbe cxgbe(4): Update T4/5/6 firmwares to 1.23.0.0. 2019-03-13 06:46:15 +00:00
dc
dcons
dcons_crom
dpms
dtb dtso: allwinner: Add an overlay for H3 thermal node 2019-08-24 13:26:34 +00:00
dtrace Disconnect fasttrap from the 32-bit powerpc build. 2019-02-21 22:49:21 +00:00
dummynet
efirt Add missing DPSRCS entry for assym.inc. 2019-06-11 23:35:49 +00:00
em Use symlinks for kernel modules rather than hardlinks 2019-04-20 12:51:05 +00:00
ena Update ENA version to v2.0.0 2019-05-30 13:52:32 +00:00
epic
epoch_test Add simple preempt safe epoch API 2018-05-10 17:55:24 +00:00
esp
et
evdev
exca
ext2fs
fdc
fdescfs
fdt Add another required header file. 2019-03-01 04:17:43 +00:00
ffec
filemon Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
firewire
firmware
fusefs Remove the fuse.ko -> fusefs.ko symlink 2019-08-07 20:28:27 +00:00
fxp Remove a use of a negative array index from fxp(4). 2018-12-19 04:54:32 +00:00
gem
geom geom_uzip(4), mkuzip(8): Add Zstd image mode 2019-08-13 23:32:56 +00:00
glxiic
glxsb
gpio
hifn
hme
hpt27xx
hptiop
hptmv
hptnr
hptrr
hwpmc Don't attempt to include hwpmc support for armv6, we're missing some of the 2019-06-12 16:05:20 +00:00
hwpmc_mips24k Add dependent header files 2019-03-28 08:30:45 +00:00
hwpmc_mips74k Add dependent header files 2019-03-28 08:30:45 +00:00
hyperv Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
i2c Add a driver for Texas Instruments ADS101x/ADS111x i2c ADC chips. 2019-08-05 15:56:44 +00:00
iavf Use symlinks for kernel modules rather than hardlinks 2019-04-20 12:51:05 +00:00
ibcore
ichwd
ida
if_bridge
if_disc
if_edsc
if_enc
if_epair
if_gif
if_gre Add GRE-in-UDP encapsulation support as defined in RFC8086. 2019-04-24 09:05:45 +00:00
if_lagg
if_me
if_ndis
if_stf
if_tuntap tun/tap: merge and rename to tuntap 2019-05-08 02:32:11 +00:00
if_vlan
if_vxlan
iflib Fix make in sys/modules 2019-03-28 08:59:11 +00:00
iir
imgact_binmisc
imx Make the imx6_snvs driver usable as a module, add pnp info. Add a manpage. 2018-07-08 19:35:41 +00:00
intelspi
io
ioat
ip6_mroute_mod
ip_mroute_mod
ipdivert
ipfilter Whitespace adjustment. 2019-06-06 03:02:25 +00:00
ipfw Rework ipfw dynamic states implementation to be lockless on fast path. 2018-02-07 18:59:54 +00:00
ipfw_nat
ipfw_nat64 Reapply r345274 with build fixes for 32-bit architectures. 2019-03-19 10:57:03 +00:00
ipfw_nptv6
ipfw_pmod
ipmi Fix a module Makefile error on amd64 so the IPMI HW interfaces are built. 2018-08-16 15:59:02 +00:00
ipoib
ips
ipsec Revert r347402. After r347429 symlink is no longer needed. 2019-05-13 08:34:13 +00:00
ipw
ipwfw
isci
iscsi
iscsi_initiator
iser Use kern.opts.mk instead of bsd.own.mk (which includes src.opts.mk) 2018-03-17 17:18:46 +00:00
isp Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
ispfw
iwi
iwifw
iwm
iwmfw Stop using .OODATE for extracting firmware. 2019-06-12 00:03:00 +00:00
iwn
iwnfw Stop using .OODATE for extracting firmware. 2019-06-12 00:03:00 +00:00
ix
ixl ixl/iavf(4): Change ixlv to iavf and update it to use iflib(9) 2018-10-12 22:40:54 +00:00
ixv
jme
kbdmux Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
kgssapi
kgssapi_krb5
khelp
krpc
ksyms
ktls_ocf Add kernel-side support for in-kernel TLS. 2019-08-27 00:01:56 +00:00
le
lge
libalias
libiconv
libmchain
lindebugfs LinuxKPI: Finalize move of lindebugfs from ports to base. 2019-05-19 15:44:21 +00:00
linprocfs Add warning to the Linuxulator makefiles that building it outside of a 2019-05-13 18:28:40 +00:00
linsysfs Add warning to the Linuxulator makefiles that building it outside of a 2019-05-13 18:28:40 +00:00
linux Replace -Werror with ${WERROR} in module builds 2019-08-25 22:06:17 +00:00
linux64 Replace -Werror with ${WERROR} in module builds 2019-08-25 22:06:17 +00:00
linux_common Add warning to the Linuxulator makefiles that building it outside of a 2019-05-13 18:28:40 +00:00
linuxkpi LinuxKPI: Finalize import of seq_file. 2019-05-16 21:17:18 +00:00
lio
lpt
mac_biba
mac_bsdextended
mac_ifoff
mac_lomac
mac_mls
mac_none
mac_ntpd Make it possible to run ntpd as a non-root user, add ntpd uid and gid. 2018-07-19 23:55:29 +00:00
mac_partition
mac_portacl
mac_seeotheruids
mac_stub
mac_test
mac_veriexec MAC/veriexec implements a verified execution environment using the MAC 2018-06-20 00:41:30 +00:00
mac_veriexec_sha1 MAC/veriexec implements a verified execution environment using the MAC 2018-06-20 00:41:30 +00:00
mac_veriexec_sha256 MAC/veriexec implements a verified execution environment using the MAC 2018-06-20 00:41:30 +00:00
mac_veriexec_sha384 MAC/veriexec implements a verified execution environment using the MAC 2018-06-20 00:41:30 +00:00
mac_veriexec_sha512 MAC/veriexec implements a verified execution environment using the MAC 2018-06-20 00:41:30 +00:00
malo
md
mdio
mem
mfi Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
mii
mlx
mlx4
mlx4en
mlx4ib
mlx5 mlx5fpga: Initial code import. 2018-12-05 14:11:20 +00:00
mlx5en Add support for Dynamic Interrupt Moderation, DIM, in mlx5en(4). 2019-05-08 10:23:33 +00:00
mlx5fpga_tools mlx5fpga_tools initial code import. 2018-12-05 14:17:22 +00:00
mlx5ib mlx5fpga: Initial code import. 2018-12-05 14:11:20 +00:00
mlxfw Initial version of Mellanox in-kernel firmware upgrade support. 2019-05-08 10:49:05 +00:00
mly
mmc
mmcnull
mmcsd
mpr Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
mps Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
mpt
mqueue Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
mrsas
msdosfs
msdosfs_iconv
msk
mthca Import the mthca kernel side infiniband driver from Linux 4.9 and fix 2018-02-13 17:04:34 +00:00
mvs
mwl
mwlfw Stop using .OODATE for extracting firmware. 2019-06-12 00:03:00 +00:00
mxge Expose zlib's utility functions in Z_SOLO library when building kernel. 2019-08-07 01:41:17 +00:00
my
nctgpio
ndis
netfpga10g
netgraph ng_ubt(4): do not attach Intel Wireless 8260/8265 in bootloader mode. 2019-08-18 22:11:42 +00:00
netmap netmap: align codebase to the current upstream (760279cfb2730a585) 2018-12-05 11:57:16 +00:00
nfe
nfscl
nfscommon Fix build in sys/modules/nfscommon 2019-04-10 16:48:45 +00:00
nfsd Add support for INET6 addresses to the kernel code that dumps open/lock state. 2019-04-13 22:00:09 +00:00
nfslock
nfslockd
nfssvc
nge
nmdm
ntb Forgotten part of r351137. 2019-08-16 20:30:31 +00:00
nullfs
nvd
nvdimm Fix make in sys/modules 2019-03-28 08:59:11 +00:00
nvme Create a AHCI attachment for nvme. 2019-08-21 22:18:01 +00:00
nvram
oce
ocs_fc Don't delete .depend files outside of cleandepend. 2019-06-12 23:09:10 +00:00
opal_nvram powerpc64/powernv: Add opal NVRAM driver for PowerNV systems 2019-09-14 03:30:34 +00:00
opensolaris Export cpu_core from opensolaris.ko. 2019-04-20 11:34:53 +00:00
otus
otusfw
ow
padlock
padlock_rng
pccard
pcfclock
pf
pflog pflog/pfsync: Fix module build with VIMAGE=yes 2018-07-01 18:09:16 +00:00
pfsync pflog/pfsync: Fix module build with VIMAGE=yes 2018-07-01 18:09:16 +00:00
plip
pms
powermac_nvram
ppbus
ppc
ppi
pps
procfs Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
proto
pseudofs
pst
pty
puc Add PNP info to the PCI attahement of the puc driver. 2018-04-17 16:46:08 +00:00
pwm Add ofw_pwmbus to enumerate pwmbus devices on systems configured with fdt 2019-06-17 03:32:05 +00:00
qlnx qlnxr(4), qlnxe(4): Unbreak gcc build 2019-02-01 23:04:45 +00:00
qlxgb
qlxgbe
qlxge
ral
ralfw Stop using .OODATE for extracting firmware. 2019-06-12 00:03:00 +00:00
random_fortuna
random_other
rc
rc4
rccgpio
rdma
rdrand_rng
re
rl
rndtest
rockchip Add RK805 PMIC Support 2018-11-28 13:53:43 +00:00
rp Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
rpi_ft5406
rtwn
rtwn_pci rtwn_pci(4): add support for RTL8188EE chipset. 2019-01-02 06:48:53 +00:00
rtwn_usb rtwn_pci(4): add support for event-based Tx reports. 2019-01-02 05:21:06 +00:00
rtwnfw Stop using .OODATE for extracting firmware. 2019-06-12 00:03:00 +00:00
s3
safe
sbni
scc
sdhci
sdhci_acpi
sdhci_pci
sdio Add opt_cam.h so we can build this outside of a kernel build. 2019-06-13 22:03:53 +00:00
sem Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
send
sfxge sfxge(4): add generated description of sensors 2018-11-30 05:54:30 +00:00
sge
sgx Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
sgx_linux
siftr
siis
sio Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
sis
sk
smartpqi smartpqi(4): Use conventional path to driver sources 2018-04-28 17:43:51 +00:00
smbfs
snp
sound Revert r338423, reapplying r338422, which did get approval but 2018-09-01 15:07:38 +00:00
speaker
spi Add opt_platform.h for several modules that have #ifdef FDT in the source. 2018-04-01 18:22:24 +00:00
spigen Fix make in sys/modules/spigen 2018-07-20 17:46:55 +00:00
splash
sppp
ste
stge
superio add superio driver 2019-07-01 17:05:41 +00:00
sym
syscons
sysvipc Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
tcp This commit updates rack to what is basically being used at NF as 2019-07-10 20:40:39 +00:00
tests
ti Add module makefiles for Texas Instruments ARM SoCs. 2019-06-16 01:22:44 +00:00
tmpfs Make TMPFS_PAGES_MINRESERVED a kernel option 2019-03-25 07:46:20 +00:00
toecore
tpm Fix make in sys/modules 2019-03-28 08:59:11 +00:00
trm
tsec
twa
twe
tws
uart add snps IP uart support / genaralize UART 2018-08-19 21:10:21 +00:00
ubsec
ubser
uchcom Set .PATH to dev/usb/serial so that these modules compile again. 2018-07-06 22:07:26 +00:00
ucycom Set .PATH to dev/usb/serial so that these modules compile again. 2018-07-06 22:07:26 +00:00
udf
udf_iconv
ufs
uinput
unionfs
usb Add cdceem(4) driver, for virtual ethernet devices compliant 2019-08-07 18:14:45 +00:00
veriexec Device for user space to interface with MAC/veriexec. 2018-06-20 00:48:46 +00:00
vesa
vge
viawd
videomode
virtio
vkbd Move most of the contents of opt_compat.h to opt_global.h. 2018-04-06 17:35:35 +00:00
vmm All genassym.sh usage need offset.inc 2018-07-03 21:02:25 +00:00
vmware Add missing dependency to vmxnet3 Makefile and clean it up a bit otherwise. 2019-01-22 04:36:19 +00:00
vnic
vpo
vr
vte
wbwd
wi
wlan
wlan_acl
wlan_amrr
wlan_ccmp
wlan_rssadapt
wlan_tkip
wlan_wep
wlan_xauth
wpi
wpifw
wtap
x86bios
xl
xz Modularize xz. 2019-02-26 19:55:03 +00:00
zfs Expose zlib's utility functions in Z_SOLO library when building kernel. 2019-08-07 01:41:17 +00:00
zlib Remove zlib 1.0.4 from kernel. 2019-08-25 17:13:00 +00:00
Makefile powerpc64/powernv: Add opal NVRAM driver for PowerNV systems 2019-09-14 03:30:34 +00:00
Makefile.inc