Lenovo ThinkStation P520 + RTX 5060Ti 16 GB - Games going in a "Bad state"

[rebelyouth.hacklab]

Hello,

I am posting this to see if someone can provide some help or some patch need to be include on the next release( or I am the only one with this issue).

I am trying to provide all the info that I have ( sorry if this will be a long post, I will summary a tl:dr at the end).

I am using Cachy OS , but I had similar issue with other distros , like Nobara and Mint and the problem that I have is :

When I got the card the driver between the 575.181 and 580.82.09 all 95% of all the game were not playable ( most of them were Windows + Proton, and some native ported games in Linux):

• low FPS (between 4 and 15 and High GPU utilization)
• broken audio ( screeching, out of sync)

To play a bit, I set the BIOS of the card to Quite mode and use the nvidia-smi and lower the speed:

nvidia-smi -lgc 1875,2650
nvidia-smi -lmc 13500

This helped a bit, but still had issue, and I tried to use X11 as was a bit better, tried to force some setting and also tried to disabled the HDMI audio ( blacklist was did not worked as the audio card use the same snd_hda_codec. Tried to use the install true as the Arch wiki suggested and I got some HDMI semi-working and the audio card, but it did not fixed the issue, so I did reverted the configuration)

---

After installed the 580.95.05 the situation changed game were finally playable even for hours ( played Control and Cyberpunk 2077 for almost all Saturday afternoon) with the following issue:

• Quitting the game to move to another or just to came back later ( see below) will result to the same problem above : low FPS (between 4 and 15 and High GPU utilization) and broken audio ( screeching, out of sync)

As I mentioned, I also discovered if I set the game on pause for more of 5 minutes, the game again behave as described above( not sure if the driver set the GPU to save mode and is not able to cameback after that).

Now with the installation of the new 580.105.08 the audio situation its better, no more broken audio ( screeching, out of sync) but issue the low FPS is still there. ( I have also Mint installed on another drive and is using the previous version 580.95.05 and the audio issue is still present)

Reboot is the only solution at the moment as I tried to restart the nvidia_drm driver but got a black screen as the system was not able to loading again the driver, so the solution was to reboot.

Btw I am using the integrated Audio card on the motherboard ( Azalia HD audio) and I also tested the HDMI out from the monitor, but I got the same results.

Never got black screen on the monitor as some post were complained and I also trying only one monitor configuration without any improvement , also the system is still working, as I can browse, also use audio for music and YouTube with the new 580.105.08 drivers , for hours, but game wise, any games that I will try to launch will present the same issues, same as any 3D application, I will just be not able to use them.

I also tried to change the pstate of the CPU set on Performance, as I was thinking that the the powersaving option) set to Balance_performance) was introducing gfx driver instability, but it did not help.

Want also to add that the video part ( Videos, Youtube) is pretty not stable as Firefox and Chrome have issue with the HW acceleration, and Smplayer have artifacts but works okyes , this will sometime ( 10 o 20% of the ) of the time corrupt the game at first start ( game will be corrupted already and reboot fixing the issue for a bit).

This is my configuration :

Host: ThinkStation P520
Kernel: Linux 6.17.8-2-cachyos
Display (ZOWIE RL LCD): 1920x1080 in 24", 60 Hz [External] *
Display (ZOWIE RL LCD): 1080x1920 in 24", 60 Hz [External]
DE: KDE Plasma 6.5.2
WM: KWin (Wayland)
WM Theme: Breeze
CPU: Intel(R) Xeon(R) W-2135 (12) @ 4.50 GHz
GPU: NVIDIA GeForce RTX 5060 Ti [Discrete]
Memory: 2.62 GiB / 62.39 GiB (4%)

The BIOS of this PC has the above 4 GB option enabled, CSM is completely off now as Secure boot, Pcie is on Gen 3.

---

inxi -GxxxZ
Graphics:
Device-1: NVIDIA GB206 [GeForce RTX 5060 Ti] vendor: Gigabyte driver: nvidia
v: 580.105.08 arch: Lovelace pcie: speed: 5 GT/s lanes: 8 ports:
active: DP-3,HDMI-A-1 empty: DP-1,DP-2 bus-ID: b3:00.0 chip-ID: 10de:2d04
class-ID: 0300
Display: wayland server: X.org v: 1.21.1.20 with: Xwayland v: 24.1.9
compositor: kwin_wayland driver: X: loaded: nvidia
gpu: nv_platform,nvidia,nvidia-nvswitch d-rect: 3840x1080 display-ID: 0
Monitor-1: DP-3 pos: right model: BenQ ZOWIE RL LCD serial: NA
res: mode: 1920x1080 hz: 60 scale: 100% (1) dpi: 92
size: 531x299mm (20.91x11.77") diag: 609mm (24") modes: max: 1920x1080
min: 640x480
Monitor-2: HDMI-A-1 pos: primary,left model: BenQ ZOWIE RL LCD
serial: NA res: mode: 1920x1080 hz: 60 scale: 178% (1.78)
to: 1080x1920 dpi: 92 size: 531x299mm (20.91x11.77") diag: 609mm (24")
modes: max: 1920x1080 min: 640x480
API: EGL v: 1.5 hw: drv: nvidia platforms: device: 0 drv: nvidia device: 2
drv: swrast gbm: drv: nvidia surfaceless: drv: nvidia wayland: drv: nvidia
x11: drv: nvidia inactive: device-1
API: OpenGL v: 4.6.0 compat-v: 4.5 vendor: nvidia mesa v: 580.105.08
glx-v: 1.4 direct-render: yes renderer: NVIDIA GeForce RTX 5060 Ti/PCIe/SSE2
display-ID: :0.0
API: Vulkan v: 1.4.328 layers: 9 surfaces: N/A device: 0
type: discrete-gpu driver: nvidia device-ID: 10de:2d04
Info: Tools: api: clinfo, eglinfo, glxinfo, vulkaninfo
de: kscreen-console,kscreen-doctor gpu: nvidia-settings,nvidia-smi
wl: wayland-info x11: xdpyinfo, xprop, xrandr

cat /etc/enviroment
QT_QPA_PLATFORM=wayland
VDPAU_DRIVER=nvidia
NVD_BACKEND=direct
LIBVA_DRIVER_NAME=nvidia-drm
MOZ_DISABLE_RDD_SANDBOX=1
__NV_PRIME_RENDER_OFFLOAD=1
__GLX_VENDOR_LIBRARY_NAME=nvidia
KWIN_DRM_ALLOW_NVIDIA_COLORSPACE=1
GBM_BACKEND=nvidia-drm
NVD_MAX_INSTANCES=2
NVD_LOG=1
__GL_SHADER_DISK_CACHE_SIZE=12000000000
PROTON_ENABLE_WAYLAND=1
CUDA_DISABLE_PERF_BOOST=1

cat /etc/modprobe.d/nvidia.conf
options nvidia-drm fbdev=1 modeset=1
options nvidia NVreg_TemporaryFilePath=/var/tmp
options nvidia NVreg_PreserveVideoMemoryAllocations=1
options nvidia NVreg_EnableMSI=0
options nvidia NVreg_EnablePCIeGen3=1
options nvidia NVreg_UsePageAttributeTable=1
options nvidia NVreg_InitializeSystemMemoryAllocations=0
options nvidia NVreg_DynamicPowerManagement=0x02
( this config look ok but idk if I introduced some options that contradict each other)

---

Here the log from yesterday session when I was playing with Control and screenshot before and after ( before good GPU and FPS and after high GPU between 70% and 99%, moat o the time at 99%, and 10 to 15 FPS, or even less)

nvidia-bug-report.log.gz (525.0 KB)

TL:DR

The card goes in a bad state and the FPS dropping and the GPU to 99%.

In the previous driver version also the audio was corrupted but with new ones that one looks fine now.

Need to reboot the PC to get the game work again, but can use the PC if I don’t want to use the 3D acceleration.

Also use HW acceleration ( video, Youtube) is causing something to get the game corrupt from the start.

---

Want also to congratulate the Nvidia team for the good work on the driver, as I can see the improvement and I hope that this ticket can improve further the stability of the drivers.

Thanks for you time and consideration,

Sincerely

Rebelyouth

[vrachatte]

I have created bug 5694850 to work on this issue.

[rebelyouth.hacklab]

Thank you

[vrachatte]

Hello @rebelyouth.hacklab, I am working on replicating this setup locally meanwhile can you just give a try on latest release driver 580.126.09 or 590.48.01. Is it possible for you to share video of this issue to understand how bad game is going. I hope this shouldn’t be system specific as on 580 we have not heard of any issue where FPS is dropping this bad or could be corner case. Lets see!!

Can you also share exact Graphics setting you have used in games? After how much time you are getting this frame drop issue?

[victor.buscsei]

Hello @rebelyouth.hacklab, Hello @vrachatte!

I also have similar if not the same issues as well in this type of PC.

I also have this Thinkstation P520 with the same Xeon W-2135 cpu and with the same amount of ram (64Gb).
The only difference is that I have a asus 5060ti DualOC.
The interesting part is that I have also experienced this similar stuttering/ laggy audio but on Win11.
This first happened after a lengthy (1-1,5 hour, with high/ultra settings) session when I played Cp2077.
The thermals were normal nothing out of ordinary and I also got this same behavior right after when I closed the game. When viewing the windows desktop the stuttering have died down but if I played a video in youtube or if I started to move the windows the stuttering have occured with sound also lagging. (Also after multiple reloads)
I have consulted with chatgpt to troubleshoot and it have recommended a few things for me:
Disable HAGs, Usual power settings change to performance with advanced power settings pcie Link State Power Management turned off.
But that still not solved it.
I also captured the latency:

Well it does not look great. So I did DDU so I will start with a clean slate, and with that (and the other mentioned settings above) did the trick.
I only installed the basic latest gameready driver (591.59) without any physx, nvidia hd audio and geforce experience. (I did not wanted to experiment installing those back or changing the hags/power settings)
Currently in win11, (with above mentioned setting changes) I do not experience such stutters and lags. Works perfectly. (Under load and also when idling)

But in the other hand, I have a dualboot with Linux mint and this is where I had more issues.
Mainly with drivers at first.
Right after I started using the 5060ti and I have booted for the first time my old linux mint OS (with kernel 5.x and probably an old driver for a 3060) I got an interlaced like output (in my second monitor only, the main monitor was in power saver mode, I guess no output was sent to that one):

Now this did not looked great :D
So I started to troubleshoot with on my side chatgpt copiloting every action:
I have booted with live usb and chroot to fix some stuff.
The old kernel to a newer 6.x one, delete the old driver and install a new one. (Also purging any xorg configs, nvidia configs, etc…)
I started with open 580.95.05 and I have stayed on that because it was displaying properly.
So with these changes I thought I was in the clear, but recently I started to notice (not exactly the same stutters what I had under win11 but similar) some video and sound stutters. For me it is frequent, every 2-5secs a stutter when idling or when under load. Also when I tried to use ai (mostly under linux I only use it for inferencing, not gaming) it have stuttered hard. So this is where I am stuck at.
What I know currently is that in my linux for some reason it downgrades the pcie to Gen2 instead of gen3.

sudo lspci -s 65:00.0 -vv | egrep -i 'LnkCap|LnkSta'
		LnkCap:	Port #0, Speed 32GT/s, Width x16, ASPM L1, Exit Latency L1 unlimited
		LnkSta:	Speed 5GT/s (downgraded), Width x8 (downgraded)
		LnkCap2: Supported Link Speeds: 2.5-32GT/s, Crosslink- Retimer+ 2Retimers+ DRS-
		LnkSta2: Current De-emphasis Level: -3.5dB, EqualizationComplete+ EqualizationPhase1+
nvidia-smi -q -d GSP_FIRMWARE_VERSION
==============NVSMI LOG============== 
Timestamp : Sun Jan 18 19:21:20 2026 
Driver Version : 580.95.05 
CUDA Version : 13.0 
Attached GPUs : 1 
GPU 00000000:65:00.0 
GSP Firmware Version : 580.95.05

Well obviously the gen2 speeds are explaining the stuttering in my understanding, and I also like to mention that I have older version of MB bios (09/19/2023) for this type of PC so multiple variables (bios, open driver, etc..) are still unknown in my case.
I know that problem is not exactly the same as what rebelyouth have shown here, but I think it still could be relevant and point to some things with our systems.
In my (not expert) opinion the pcie could be the main troublemaker. I think this motherboard (or at least mine) does not handle any pcie gen changes gracefully under linux.
In win11 I saw that during load it will upgrade the connection to gen3 and when idling it will go to pcie gen 1.1 or gen2.
Now I don’t want to point to some things. I am not an expert here and I also don’t want to deviate the discussion about rebelyouth problem, but I still think that these cases somehow could be linked.

Please vrachatte, do what you need to do and if you think that my issue is not connected in any way possible, I will create a new thread.
I just wanted to add some additional information from my experience with the same HW.
(At least this comment maybe, could help someone who is in the same shoes)

Thank you in advance for your work vrachatte and also thank you rebelyouth for creating this thread.

I will let you know here if I experiment with some stuff and if that has any affect to the issues I have experienced.

Kind regards,
Viktor

[victor.buscsei]

Hello,

I am back with some updates.
Unfortunately not with good ones.
So I have updated my bios to the latest, all the other things as well (intel me, chipset, etc.) and on the windows side everything have worked normally. No issues, no weird stutters or anything. Smooth normal working card.
But on the linux side where I had most of the issues nothing have happened. The same behavior.
After that I have upgraded my linux mint from 21 to 21.3.
Nothing have changed.
After that from 21.3 to 22 (which based on ubuntu 24.04 with kernel 6.8.0-90-generic).
Same, nothing have changed. Maybe a little because it could stay normal for half an hour or maybe an hour but after that it will go to this gen2 and stays there with stutters and everything.
At this point I am with 590.48.01 drivers but the issues still appear.
After that I have upgraded to the latest 22.3 version of linux mint.
Everything is the same. I also tried to change my kernel to 6.14 but that did not change anything.

I tested also a little bit and it seems that it needs some kind of a load and after the load a little bit it will stay in gen 3 or switch to gen 2 and back to gen 3 but it will eventually go to gen 2 with some random spikes in the gpu util.:

Also after this gen2 stuck state it will eat 10w plus what should have been baseline without load ( around ~20w or so)

I also disabled secure boot, but nothing have changed.

So I am out of options really. I tried everything but nothing works.

The earlier capture is from the linux mint 22 and the latest one from 22.3.
Both with 590.48.01.
I also captured some other outputs with some which was continous with timestamps when the swithes from gen2 to gen3 and vice versa happens.
nvidia_pcie_drop_2026-01-25_125817.tar.gz (565.1 KB)
nvidia_pcie_drop_2026-01-25_184459.tar.gz (2.4 MB)

@vrachatte could you take a look at it?
What options would you recommend?

Thank you in advance.
Kind regards,
Viktor

[verjoz]

Hi Victor, Rebelyouth and Vrachatte,

I just purchased 2x5060 Ti 16GB, and having the EXACT SAME issue:

• after some time, the card slows down a LOT, and only reboot helps
• same symptom that instead of max Gen3 (that initially I have) goes only to Gen2 max

Config:

• Same ThinkStation P520 (same CPU + same 64Gb Ram)
• Ubuntu 24.04
• driver 580.95.05 (open)

Usecase:

• AI infer small LLM (NVIDIA Nemotron 3 Nano)
• For some time runs OK, then slows down 10x :(

vrachatte Your help would be really appreciated.

Thank you in advance,

[vrachatte]

@rebelyouth.hacklab can you please check and update on above asked query?

[yonnibanin]

Hi,

I am reporting the exact same issue on a Lenovo ThinkStation P520 (Xeon W-2135) with an ASUS Prime RTX 5060 8GB (Driver 581.57 / Studio).

I’ve attached an HWiNFO64 log that clearly captures the “Bad State” mentioned in this thread.

Key observations from my logs:

• PCIe Link Speed Anomaly: The card frequently struggles to maintain Gen 3 speeds and exhibits severe stuttering (low FPS/high latency) when VRAM usage nears 7.7GB.

• VRAM Saturation Trigger: Even in “Low” settings in MSFS, once VRAM hits the 7.8GB-8GB threshold, the system latency spikes to 140ms+ and FPS drops to single digits.

• Temporary Recovery: In some cases, once VRAM allocation drops back to ~7.3GB, the card “wakes up” and performance jumps from 15 FPS to 45 FPS instantly.

• VR Instability: The issue is catastrophic in VR (Oculus Link), where the frame delivery completely breaks down regardless of in-game settings.

I see that Bug 5694850 has been created for this. If you need any specific tests or BIOS/VBIOS dumps from a P520 user, please let me know. I am happy to assist in resolving this compatibility issue.

Thank you!

The HWiNFO CSV File:

HWiNFO afterstartup.CSV

[verjoz]

Hi @vrachatte,

Can you progress without @rebelyouth.hacklab ?
@yonnibanin also just reported the exact same issue..

Your prompt reply would be really appreciated, as this seems to be an issue open for close to half an year :(

[vrachatte]

Can you share o/p of “lspci -vv -s 01:00.0 | grep LnkSta“ from your system?

[verjoz]

Hi @vrachatte,

Thank you for your follow up//prompt reply!

$ lspci -vv -s 01:00.0 | grep LnkSta
gives nothing, as no 01:00.0 (see below the full lspci output)

(now i am in a rebooted OK so not in the bad state)

$ lspci -vv
00:00.0 Host bridge: Intel Corporation Sky Lake-E DMI3 Registers (rev 04)
Subsystem: Lenovo Sky Lake-E DMI3 Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Interrupt: pin A routed to IRQ 0
NUMA node: 0
IOMMU group: 6
Capabilities:

00:04.0 System peripheral: Intel Corporation Sky Lake-E CBDMA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CBDMA Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 77
NUMA node: 0
IOMMU group: 7
Region 0: Memory at 43ffff30000 (64-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: ioatdma
Kernel modules: ioatdma

00:04.1 System peripheral: Intel Corporation Sky Lake-E CBDMA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CBDMA Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin B routed to IRQ 79
NUMA node: 0
IOMMU group: 8
Region 0: Memory at 43ffff2c000 (64-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: ioatdma
Kernel modules: ioatdma

00:04.2 System peripheral: Intel Corporation Sky Lake-E CBDMA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CBDMA Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin C routed to IRQ 77
NUMA node: 0
IOMMU group: 9
Region 0: Memory at 43ffff28000 (64-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: ioatdma
Kernel modules: ioatdma

00:04.3 System peripheral: Intel Corporation Sky Lake-E CBDMA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CBDMA Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin D routed to IRQ 79
NUMA node: 0
IOMMU group: 10
Region 0: Memory at 43ffff24000 (64-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: ioatdma
Kernel modules: ioatdma

00:04.4 System peripheral: Intel Corporation Sky Lake-E CBDMA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CBDMA Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 77
NUMA node: 0
IOMMU group: 11
Region 0: Memory at 43ffff20000 (64-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: ioatdma
Kernel modules: ioatdma

00:04.5 System peripheral: Intel Corporation Sky Lake-E CBDMA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CBDMA Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin B routed to IRQ 79
NUMA node: 0
IOMMU group: 12
Region 0: Memory at 43ffff1c000 (64-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: ioatdma
Kernel modules: ioatdma

00:04.6 System peripheral: Intel Corporation Sky Lake-E CBDMA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CBDMA Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin C routed to IRQ 77
NUMA node: 0
IOMMU group: 13
Region 0: Memory at 43ffff18000 (64-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: ioatdma
Kernel modules: ioatdma

00:04.7 System peripheral: Intel Corporation Sky Lake-E CBDMA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CBDMA Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin D routed to IRQ 79
NUMA node: 0
IOMMU group: 14
Region 0: Memory at 43ffff14000 (64-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: ioatdma
Kernel modules: ioatdma

00:05.0 System peripheral: Intel Corporation Sky Lake-E MM/Vt-d Configuration Registers (rev 04)
Subsystem: Lenovo Sky Lake-E MM/Vt-d Configuration Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 15
Capabilities:

00:05.2 System peripheral: Intel Corporation Sky Lake-E RAS (rev 04)
Subsystem: Lenovo Sky Lake-E RAS
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 16
Capabilities:

00:05.4 PIC: Intel Corporation Sky Lake-E IOAPIC (rev 04) (prog-if 20 [IO(X)-APIC])
Subsystem: Lenovo Sky Lake-E IOAPIC
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
NUMA node: 0
IOMMU group: 17
Region 0: Memory at 90339000 (32-bit, non-prefetchable) [size=4K]
Capabilities:

00:08.0 System peripheral: Intel Corporation Sky Lake-E Ubox Registers (rev 04)
Subsystem: Lenovo Sky Lake-E Ubox Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 18
Capabilities:

00:08.1 Performance counters: Intel Corporation Sky Lake-E Ubox Registers (rev 04)
Subsystem: Lenovo Sky Lake-E Ubox Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 19

00:08.2 System peripheral: Intel Corporation Sky Lake-E Ubox Registers (rev 04)
Subsystem: Lenovo Sky Lake-E Ubox Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 20
Capabilities:

00:14.0 USB controller: Intel Corporation 200 Series/Z370 Chipset Family USB 3.0 xHCI Controller (prog-if 30 [XHCI])
Subsystem: Lenovo 200 Series/Z370 Chipset Family USB 3.0 xHCI Controller
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B+ ParErr- DEVSEL=medium >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0
Interrupt: pin A routed to IRQ 34
NUMA node: 0
IOMMU group: 21
Region 0: Memory at 90320000 (64-bit, non-prefetchable) [size=64K]
Capabilities:
Kernel driver in use: xhci_hcd
Kernel modules: xhci_pci

00:14.2 Signal processing controller: Intel Corporation 200 Series PCH Thermal Subsystem
Subsystem: Lenovo 200 Series PCH Thermal Subsystem
Control: I/O- Mem+ BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Interrupt: pin C routed to IRQ 255
NUMA node: 0
IOMMU group: 21
Region 0: Memory at 43ffff37000 (64-bit, non-prefetchable) [size=4K]
Capabilities:

00:16.0 Communication controller: Intel Corporation 200 Series PCH CSME HECI #1
Subsystem: Lenovo 200 Series PCH CSME HECI
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0
Interrupt: pin A routed to IRQ 87
NUMA node: 0
IOMMU group: 22
Region 0: Memory at 43ffff36000 (64-bit, non-prefetchable) [size=4K]
Capabilities:
Kernel driver in use: mei_me
Kernel modules: mei_me

00:16.3 Serial controller: Intel Corporation 200 Series Chipset Family KT Redirection (prog-if 02 [16550])
Subsystem: Lenovo Device 1036
Control: I/O+ Mem+ BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz+ UDF- FastB2B+ ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Interrupt: pin D routed to IRQ 19
NUMA node: 0
IOMMU group: 22
Region 0: I/O ports at 3060 [size=8]
Region 1: Memory at 90338000 (32-bit, non-prefetchable) [size=4K]
Capabilities:
Kernel driver in use: serial

00:17.0 SATA controller: Intel Corporation 200 Series PCH SATA controller [AHCI mode] (prog-if 01 [AHCI 1.0])
Subsystem: Lenovo 200 Series PCH SATA controller [AHCI mode]
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz+ UDF- FastB2B+ ParErr- DEVSEL=medium >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0
Interrupt: pin A routed to IRQ 42
NUMA node: 0
IOMMU group: 23
Region 0: Memory at 90334000 (32-bit, non-prefetchable) [size=8K]
Region 1: Memory at 90337000 (32-bit, non-prefetchable) [size=256]
Region 2: I/O ports at 3050 [size=8]
Region 3: I/O ports at 3040 [size=4]
Region 4: I/O ports at 3020 [size=32]
Region 5: Memory at 90336000 (32-bit, non-prefetchable) [size=2K]
Capabilities:
Kernel driver in use: ahci
Kernel modules: ahci

00:1b.0 PCI bridge: Intel Corporation 200 Series PCH PCI Express Root Port #17 (rev f0) (prog-if 00 [Normal decode])
Subsystem: Lenovo 200 Series PCH PCI Express Root Port
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 24
NUMA node: 0
IOMMU group: 24
Bus: primary=00, secondary=01, subordinate=01, sec-latency=0
I/O behind bridge: [disabled] [16-bit]
Memory behind bridge: [disabled] [32-bit]
Prefetchable memory behind bridge: [disabled] [64-bit]
Secondary status: 66MHz- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- <MAbort+ <SERR- <PERR-
BridgeCtl: Parity- SERR+ NoISA- VGA- VGA16+ MAbort- >Reset- FastB2B-
PriDiscTmr- SecDiscTmr- DiscTmrStat- DiscTmrSERREn-
Capabilities:
Kernel driver in use: pcieport

00:1b.4 PCI bridge: Intel Corporation 200 Series PCH PCI Express Root Port #21 (rev f0) (prog-if 00 [Normal decode])
Subsystem: Lenovo 200 Series PCH PCI Express Root Port
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 25
NUMA node: 0
IOMMU group: 25
Bus: primary=00, secondary=02, subordinate=02, sec-latency=0
I/O behind bridge: [disabled] [16-bit]
Memory behind bridge: 90200000-902fffff [size=1M] [32-bit]
Prefetchable memory behind bridge: [disabled] [64-bit]
Secondary status: 66MHz- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- <MAbort+ <SERR- <PERR-
BridgeCtl: Parity+ SERR+ NoISA- VGA- VGA16+ MAbort- >Reset- FastB2B-
PriDiscTmr- SecDiscTmr- DiscTmrStat- DiscTmrSERREn-
Capabilities:
Kernel driver in use: pcieport

00:1d.0 PCI bridge: Intel Corporation 200 Series PCH PCI Express Root Port #9 (rev f0) (prog-if 00 [Normal decode])
Subsystem: Lenovo 200 Series PCH PCI Express Root Port
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 26
NUMA node: 0
IOMMU group: 26
Bus: primary=00, secondary=03, subordinate=03, sec-latency=0
I/O behind bridge: 1000-1fff [size=4K] [16-bit]
Memory behind bridge: fdd00000-fdefffff [size=2M] [32-bit]
Prefetchable memory behind bridge: 40000000000-400001fffff [size=2M] [32-bit]
Secondary status: 66MHz- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- <MAbort+ <SERR- <PERR-
BridgeCtl: Parity- SERR+ NoISA- VGA- VGA16+ MAbort- >Reset- FastB2B-
PriDiscTmr- SecDiscTmr- DiscTmrStat- DiscTmrSERREn-
Capabilities:
Kernel driver in use: pcieport

00:1d.2 PCI bridge: Intel Corporation 200 Series PCH PCI Express Root Port #11 (rev f0) (prog-if 00 [Normal decode])
Subsystem: Lenovo 200 Series PCH PCI Express Root Port
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin C routed to IRQ 27
NUMA node: 0
IOMMU group: 27
Bus: primary=00, secondary=04, subordinate=05, sec-latency=0
I/O behind bridge: [disabled] [16-bit]
Memory behind bridge: [disabled] [32-bit]
Prefetchable memory behind bridge: [disabled] [64-bit]
Secondary status: 66MHz- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- <MAbort+ <SERR- <PERR-
BridgeCtl: Parity+ SERR+ NoISA- VGA- VGA16+ MAbort- >Reset- FastB2B-
PriDiscTmr- SecDiscTmr- DiscTmrStat- DiscTmrSERREn-
Capabilities:
Kernel driver in use: pcieport

00:1e.0 Signal processing controller: Intel Corporation 200 Series/Z370 Chipset Family Serial IO UART Controller #0
Subsystem: Lenovo 200 Series/Z370 Chipset Family Serial IO UART Controller
Control: I/O- Mem+ BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Interrupt: pin A routed to IRQ -2147483648
NUMA node: 0
IOMMU group: 28
Region 0: Memory at 43ffff35000 (64-bit, non-prefetchable) [size=4K]
Capabilities:
Kernel modules: intel_lpss_pci

00:1f.0 ISA bridge: Intel Corporation C422 Chipset LPC/eSPI Controller
Subsystem: Lenovo C422 Chipset LPC/eSPI Controller
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=medium >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0
NUMA node: 0
IOMMU group: 29

00:1f.2 Memory controller: Intel Corporation 200 Series/Z370 Chipset Family Power Management Controller
Subsystem: Lenovo 200 Series/Z370 Chipset Family Power Management Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 29
Region 0: Memory at 90330000 (32-bit, non-prefetchable) [disabled] [size=16K]

00:1f.3 Audio device: Intel Corporation 200 Series PCH HD Audio
Subsystem: Lenovo 200 Series PCH HD Audio
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 32, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 90
NUMA node: 0
IOMMU group: 29
Region 0: Memory at 43ffff10000 (64-bit, non-prefetchable) [size=16K]
Region 4: Memory at 43ffff00000 (64-bit, non-prefetchable) [size=64K]
Capabilities:
Kernel driver in use: snd_hda_intel
Kernel modules: snd_hda_intel, snd_soc_avs

00:1f.4 SMBus: Intel Corporation 200 Series/Z370 Chipset Family SMBus Controller
Subsystem: Lenovo 200 Series/Z370 Chipset Family SMBus Controller
Control: I/O+ Mem+ BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B+ ParErr- DEVSEL=medium >TAbort- <TAbort- SERR- <PERR- INTx-
Interrupt: pin A routed to IRQ 16
NUMA node: 0
IOMMU group: 29
Region 0: Memory at 43ffff34000 (64-bit, non-prefetchable) [size=256]
Region 4: I/O ports at 3000 [size=32]
Kernel driver in use: i801_smbus
Kernel modules: i2c_i801

00:1f.6 Ethernet controller: Intel Corporation Ethernet Connection (2) I219-LM
DeviceName: i219
Subsystem: Lenovo Ethernet Connection (2) I219-LM
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0
Interrupt: pin D routed to IRQ 33
NUMA node: 0
IOMMU group: 30
Region 0: Memory at 90300000 (32-bit, non-prefetchable) [size=128K]
Capabilities:
Kernel driver in use: e1000e
Kernel modules: e1000e

02:00.0 USB controller: ASMedia Technology Inc. ASM1142 USB 3.1 Host Controller (prog-if 30 [XHCI])
Subsystem: Lenovo ASM1142 USB 3.1 Host Controller
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 16
NUMA node: 0
IOMMU group: 31
Region 0: Memory at 90200000 (64-bit, non-prefetchable) [size=32K]
Capabilities:
Kernel driver in use: xhci_hcd
Kernel modules: xhci_pci

04:00.0 PCI bridge: Pericom Semiconductor PI7C9X113SL/PI7C9X118SL PCIe-to-PCI Bridge (prog-if 00 [Normal decode])
Control: I/O+ Mem+ BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Interrupt: pin A routed to IRQ 255
NUMA node: 0
IOMMU group: 32
Bus: primary=04, secondary=05, subordinate=05, sec-latency=64
I/O behind bridge: [disabled] [32-bit]
Memory behind bridge: [disabled] [32-bit]
Prefetchable memory behind bridge: [disabled] [64-bit]
Secondary status: 66MHz+ FastB2B+ ParErr- DEVSEL=medium >TAbort- <TAbort- <MAbort+ <SERR- <PERR-
BridgeCtl: Parity+ SERR+ NoISA- VGA- VGA16+ MAbort- >Reset- FastB2B-
PriDiscTmr- SecDiscTmr- DiscTmrStat- DiscTmrSERREn-
Capabilities:

16:00.0 PCI bridge: Intel Corporation Sky Lake-E PCI Express Root Port A (rev 04) (prog-if 00 [Normal decode])
Subsystem: Lenovo Sky Lake-E PCI Express Root Port A
Physical Slot: 4
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 29
NUMA node: 0
IOMMU group: 2
Bus: primary=16, secondary=17, subordinate=17, sec-latency=0
I/O behind bridge: 7000-7fff [size=4K] [16-bit]
Memory behind bridge: 94000000-980fffff [size=65M] [32-bit]
Prefetchable memory behind bridge: 44000000000-4402fffffff [size=768M] [32-bit]
Secondary status: 66MHz- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- <MAbort+ <SERR- <PERR-
BridgeCtl: Parity+ SERR+ NoISA- VGA- VGA16+ MAbort- >Reset- FastB2B-
PriDiscTmr- SecDiscTmr- DiscTmrStat- DiscTmrSERREn-
Capabilities:
Kernel driver in use: pcieport

16:02.0 PCI bridge: Intel Corporation Sky Lake-E PCI Express Root Port C (rev 04) (prog-if 00 [Normal decode])
Subsystem: Lenovo Sky Lake-E PCI Express Root Port C
Physical Slot: 0
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 30
NUMA node: 0
IOMMU group: 3
Bus: primary=16, secondary=18, subordinate=18, sec-latency=0
I/O behind bridge: [disabled] [16-bit]
Memory behind bridge: 98100000-981fffff [size=1M] [32-bit]
Prefetchable memory behind bridge: [disabled] [64-bit]
Secondary status: 66MHz- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- <MAbort+ <SERR- <PERR-
BridgeCtl: Parity+ SERR+ NoISA- VGA- VGA16+ MAbort- >Reset- FastB2B-
PriDiscTmr- SecDiscTmr- DiscTmrStat- DiscTmrSERREn-
Capabilities:
Kernel driver in use: pcieport

16:05.0 System peripheral: Intel Corporation Sky Lake-E VT-d (rev 04)
Subsystem: Lenovo Sky Lake-E VT-d
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 33
Capabilities:

16:05.2 System peripheral: Intel Corporation Sky Lake-E RAS Configuration Registers (rev 04)
Subsystem: Lenovo Sky Lake-E RAS Configuration Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 34
Capabilities:

16:05.4 PIC: Intel Corporation Sky Lake-E IOxAPIC Configuration Registers (rev 04) (prog-if 20 [IO(X)-APIC])
Subsystem: Lenovo Sky Lake-E IOxAPIC Configuration Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
NUMA node: 0
IOMMU group: 35
Region 0: Memory at 98200000 (32-bit, non-prefetchable) [size=4K]
Capabilities:

16:08.0 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 36

16:08.1 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 36

16:08.2 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 36

16:08.3 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 36

16:08.4 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 36

16:08.5 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 36

16:08.6 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 36

16:08.7 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 36

16:09.0 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 37

16:09.1 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 37

16:0e.0 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 38

16:0e.1 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 38

16:0e.2 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 38

16:0e.3 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 38

16:0e.4 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 38

16:0e.5 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 38

16:0e.6 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 38

16:0e.7 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 38

16:0f.0 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 39

16:0f.1 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 39

16:1d.0 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 40

16:1d.1 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 40

16:1d.2 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 40

16:1d.3 System peripheral: Intel Corporation Sky Lake-E CHA Registers (rev 04)
Subsystem: Lenovo Sky Lake-E CHA Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 40

16:1e.0 System peripheral: Intel Corporation Sky Lake-E PCU Registers (rev 04)
Subsystem: Lenovo Sky Lake-E PCU Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 41

16:1e.1 System peripheral: Intel Corporation Sky Lake-E PCU Registers (rev 04)
Subsystem: Lenovo Sky Lake-E PCU Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 41

16:1e.2 System peripheral: Intel Corporation Sky Lake-E PCU Registers (rev 04)
Subsystem: Lenovo Sky Lake-E PCU Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 41

16:1e.3 System peripheral: Intel Corporation Sky Lake-E PCU Registers (rev 04)
Subsystem: Lenovo Sky Lake-E PCU Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 41

16:1e.4 System peripheral: Intel Corporation Sky Lake-E PCU Registers (rev 04)
Subsystem: Lenovo Sky Lake-E PCU Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 41

16:1e.5 System peripheral: Intel Corporation Sky Lake-E PCU Registers (rev 04)
Subsystem: Lenovo Sky Lake-E PCU Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 41

16:1e.6 System peripheral: Intel Corporation Sky Lake-E PCU Registers (rev 04)
Subsystem: Lenovo Sky Lake-E PCU Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 41

17:00.0 VGA compatible controller: NVIDIA Corporation Device 2d04 (rev a1) (prog-if 00 [VGA controller])
Subsystem: Gigabyte Technology Co., Ltd Device 418f
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0
Interrupt: pin A routed to IRQ 88
NUMA node: 0
IOMMU group: 4
Region 0: Memory at 94000000 (32-bit, non-prefetchable) [size=64M]
Region 1: Memory at 44000000000 (64-bit, prefetchable) [size=256M]
Region 3: Memory at 44020000000 (64-bit, prefetchable) [size=32M]
Region 5: I/O ports at 7000 [size=128]
Expansion ROM at 98000000 [virtual] [disabled] [size=512K]
Capabilities:
Kernel driver in use: nvidia
Kernel modules: nvidiafb, nouveau, nvidia_drm, nvidia

17:00.1 Audio device: NVIDIA Corporation Device 22eb (rev a1)
Subsystem: NVIDIA Corporation Device 0000
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR+ FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 32 bytes
Interrupt: pin B routed to IRQ 91
NUMA node: 0
IOMMU group: 4
Region 0: Memory at 98080000 (32-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: snd_hda_intel
Kernel modules: snd_hda_intel

18:00.0 Non-Volatile memory controller: Samsung Electronics Co Ltd NVMe SSD Controller SM981/PM981/PM983 (prog-if 02 [NVM Express])
Subsystem: Samsung Electronics Co Ltd SSD 970 EVO/PRO
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 32 bytes
Interrupt: pin A routed to IRQ 46
NUMA node: 0
IOMMU group: 5
Region 0: Memory at 98100000 (64-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: nvme
Kernel modules: nvme

64:05.0 System peripheral: Intel Corporation Sky Lake-E VT-d (rev 04)
Subsystem: Lenovo Sky Lake-E VT-d
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 42
Capabilities:

64:05.2 System peripheral: Intel Corporation Sky Lake-E RAS Configuration Registers (rev 04)
Subsystem: Lenovo Sky Lake-E RAS Configuration Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 43
Capabilities:

64:05.4 PIC: Intel Corporation Sky Lake-E IOxAPIC Configuration Registers (rev 04) (prog-if 20 [IO(X)-APIC])
Subsystem: Lenovo Sky Lake-E IOxAPIC Configuration Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
NUMA node: 0
IOMMU group: 44
Region 0: Memory at b3300000 (32-bit, non-prefetchable) [size=4K]
Capabilities:

64:08.0 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 45
Capabilities:
Kernel driver in use: skx_uncore

64:09.0 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 46
Capabilities:
Kernel driver in use: skx_uncore

64:0a.0 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 47
Capabilities:

64:0a.1 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 48
Capabilities:

64:0a.2 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 49
Capabilities:
Kernel driver in use: skx_uncore

64:0a.3 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 50
Capabilities:

64:0a.4 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 51
Capabilities:

64:0a.5 System peripheral: Intel Corporation Sky Lake-E LM Channel 1 (rev 04)
Subsystem: Lenovo Sky Lake-E LM Channel 1
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 52
Capabilities:

64:0a.6 System peripheral: Intel Corporation Sky Lake-E LMS Channel 1 (rev 04)
Subsystem: Lenovo Sky Lake-E LMS Channel 1
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 53
Capabilities:
Kernel driver in use: skx_uncore

64:0a.7 System peripheral: Intel Corporation Sky Lake-E LMDP Channel 1 (rev 04)
Subsystem: Lenovo Sky Lake-E LMDP Channel 1
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 54
Capabilities:

64:0b.0 System peripheral: Intel Corporation Sky Lake-E DECS Channel 2 (rev 04)
Subsystem: Lenovo Sky Lake-E DECS Channel 2
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 55
Capabilities:

64:0b.1 System peripheral: Intel Corporation Sky Lake-E LM Channel 2 (rev 04)
Subsystem: Lenovo Sky Lake-E LM Channel 2
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 56
Capabilities:

64:0b.2 System peripheral: Intel Corporation Sky Lake-E LMS Channel 2 (rev 04)
Subsystem: Lenovo Sky Lake-E LMS Channel 2
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 57
Capabilities:
Kernel driver in use: skx_uncore

64:0b.3 System peripheral: Intel Corporation Sky Lake-E LMDP Channel 2 (rev 04)
Subsystem: Lenovo Sky Lake-E LMDP Channel 2
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 58
Capabilities:

64:0c.0 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 59
Capabilities:

64:0c.1 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 60
Capabilities:

64:0c.2 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 61
Capabilities:
Kernel driver in use: skx_uncore

64:0c.3 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 62
Capabilities:

64:0c.4 System peripheral: Intel Corporation Sky Lake-E Integrated Memory Controller (rev 04)
Subsystem: Lenovo Sky Lake-E Integrated Memory Controller
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 63
Capabilities:

64:0c.5 System peripheral: Intel Corporation Sky Lake-E LM Channel 1 (rev 04)
Subsystem: Lenovo Sky Lake-E LM Channel 1
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 64
Capabilities:

64:0c.6 System peripheral: Intel Corporation Sky Lake-E LMS Channel 1 (rev 04)
Subsystem: Lenovo Sky Lake-E LMS Channel 1
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 65
Capabilities:
Kernel driver in use: skx_uncore

64:0c.7 System peripheral: Intel Corporation Sky Lake-E LMDP Channel 1 (rev 04)
Subsystem: Lenovo Sky Lake-E LMDP Channel 1
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 66
Capabilities:

64:0d.0 System peripheral: Intel Corporation Sky Lake-E DECS Channel 2 (rev 04)
Subsystem: Lenovo Sky Lake-E DECS Channel 2
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 67
Capabilities:

64:0d.1 System peripheral: Intel Corporation Sky Lake-E LM Channel 2 (rev 04)
Subsystem: Lenovo Sky Lake-E LM Channel 2
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 68
Capabilities:

64:0d.2 System peripheral: Intel Corporation Sky Lake-E LMS Channel 2 (rev 04)
Subsystem: Lenovo Sky Lake-E LMS Channel 2
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 69
Capabilities:
Kernel driver in use: skx_uncore

64:0d.3 System peripheral: Intel Corporation Sky Lake-E LMDP Channel 2 (rev 04)
Subsystem: Lenovo Sky Lake-E LMDP Channel 2
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 70
Capabilities:

b2:00.0 PCI bridge: Intel Corporation Sky Lake-E PCI Express Root Port A (rev 04) (prog-if 00 [Normal decode])
Subsystem: Lenovo Sky Lake-E PCI Express Root Port A
Physical Slot: 1
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr+ Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
Interrupt: pin A routed to IRQ 32
NUMA node: 0
IOMMU group: 0
Bus: primary=b2, secondary=b3, subordinate=b3, sec-latency=0
I/O behind bridge: f000-ffff [size=4K] [16-bit]
Memory behind bridge: f4000000-f80fffff [size=65M] [32-bit]
Prefetchable memory behind bridge: 4c000000000-4c02fffffff [size=768M] [32-bit]
Secondary status: 66MHz- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- <MAbort+ <SERR- <PERR-
BridgeCtl: Parity+ SERR+ NoISA- VGA- VGA16+ MAbort- >Reset- FastB2B-
PriDiscTmr- SecDiscTmr- DiscTmrStat- DiscTmrSERREn-
Capabilities:
Kernel driver in use: pcieport

b2:05.0 System peripheral: Intel Corporation Sky Lake-E VT-d (rev 04)
Subsystem: Lenovo Sky Lake-E VT-d
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 71
Capabilities:

b2:05.2 System peripheral: Intel Corporation Sky Lake-E RAS Configuration Registers (rev 04)
Subsystem: Lenovo Sky Lake-E RAS Configuration Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 72
Capabilities:

b2:05.4 PIC: Intel Corporation Sky Lake-E IOxAPIC Configuration Registers (rev 04) (prog-if 20 [IO(X)-APIC])
Subsystem: Lenovo Sky Lake-E IOxAPIC Configuration Registers
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 64 bytes
NUMA node: 0
IOMMU group: 73
Region 0: Memory at f8100000 (32-bit, non-prefetchable) [size=4K]
Capabilities:

b2:12.0 Performance counters: Intel Corporation Sky Lake-E M3KTI Registers (rev 04)
Subsystem: Lenovo Sky Lake-E M3KTI Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 74
Capabilities:

b2:12.1 Performance counters: Intel Corporation Sky Lake-E M3KTI Registers (rev 04)
Subsystem: Lenovo Sky Lake-E M3KTI Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 75
Kernel driver in use: skx_uncore

b2:12.2 System peripheral: Intel Corporation Sky Lake-E M3KTI Registers (rev 04)
Subsystem: Lenovo Sky Lake-E M3KTI Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 75
Kernel driver in use: skx_uncore

b2:15.0 System peripheral: Intel Corporation Sky Lake-E M2PCI Registers (rev 04)
Subsystem: Lenovo Sky Lake-E M2PCI Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 76

b2:16.0 System peripheral: Intel Corporation Sky Lake-E M2PCI Registers (rev 04)
Subsystem: Lenovo Sky Lake-E M2PCI Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 77

b2:16.4 System peripheral: Intel Corporation Sky Lake-E M2PCI Registers (rev 04)
Subsystem: Lenovo Sky Lake-E M2PCI Registers
Control: I/O- Mem- BusMaster- SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
Status: Cap- 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
NUMA node: 0
IOMMU group: 77

b3:00.0 VGA compatible controller: NVIDIA Corporation Device 2d04 (rev a1) (prog-if 00 [VGA controller])
Subsystem: Micro-Star International Co., Ltd. [MSI] Device 5351
Control: I/O+ Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR+ FastB2B- DisINTx+
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0
Interrupt: pin A routed to IRQ 89
NUMA node: 0
IOMMU group: 1
Region 0: Memory at f4000000 (32-bit, non-prefetchable) [size=64M]
Region 1: Memory at 4c000000000 (64-bit, prefetchable) [size=256M]
Region 3: Memory at 4c020000000 (64-bit, prefetchable) [size=32M]
Region 5: I/O ports at f000 [size=128]
Expansion ROM at f8000000 [virtual] [disabled] [size=512K]
Capabilities:
Kernel driver in use: nvidia
Kernel modules: nvidiafb, nouveau, nvidia_drm, nvidia

b3:00.1 Audio device: NVIDIA Corporation Device 22eb (rev a1)
Subsystem: NVIDIA Corporation Device 0000
Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR+ FastB2B- DisINTx-
Status: Cap+ 66MHz- UDF- FastB2B- ParErr- DEVSEL=fast >TAbort- <TAbort- SERR- <PERR- INTx-
Latency: 0, Cache Line Size: 32 bytes
Interrupt: pin B routed to IRQ 92
NUMA node: 0
IOMMU group: 1
Region 0: Memory at f8080000 (32-bit, non-prefetchable) [size=16K]
Capabilities:
Kernel driver in use: snd_hda_intel
Kernel modules: snd_hda_intel

[vrachatte]

Thanks for the output. Can you run below command and share output:

sudo lspci -vv -s 17:00.0 | grep -E ‘LnkCap|LnkSta’
sudo lspci -vv -s 16:00.0 | grep -E ‘LnkCap|LnkSta’

sudo lspci -vv -s b3:00.0 | grep -E ‘LnkCap|LnkSta’
sudo lspci -vv -s b2:00.0 | grep -E ‘LnkCap|LnkSta’

Basically I want to understand what is PCI speed where Nvidia card is connected, is it PCIe x16 or PCIe x 8 and what is bandwidth values?

[verjoz]

Hi @vrachatte,

A week ago I think I managed to fix the issue (I just wanted to wait for the test to make sure it is ok):

• using 580.126.0.9 … AND
• running a tiny constant GPU load on BOTH GPUs seems to solve the issue

Tiny load:

• I used this .cu program to run ALWAYS in the background:

1.) create keepalive.cu file:

include <cuda_runtime.h>
include <unistd.h>
include <stdio.h>
include <stdlib.h>

int main() {
int n = 0;
cudaGetDeviceCount(&n);
if (n <= 0) return 1;

void **ptrs = (void**)calloc(n, sizeof(void*));
for (int i = 0; i < n; i++) {
    cudaSetDevice(i);
    cudaMalloc(&ptrs[i], 4);
}

while (1) {
    for (int i = 0; i < n; i++) {
        cudaSetDevice(i);
        cudaMemset(ptrs[i], 0, 4);
    }
    for (int i = 0; i < n; i++) {
        cudaSetDevice(i);
        cudaDeviceSynchronize();
    }
    usleep(100000);
}

return 0;

}

2.) then compile:
nvcc -o keepalive keepalive.cu

3.) then run it (always start on bootup):
*./keepalive

This only uses 130MB of VRAM and negligable GPU Utilization:

I hope this could help others as well. :)

[crueltuner]

I have had issues. But mine is totally freezing. You had solution but why its doing that. Is just older version of driver anyu good for solution?