* GPU hang trying to run OpenCL kernels on x86_64
@ 2018-05-04 16:27 Luís Mendes
[not found] ` <CAEzXK1p3SnOnduP0nL1D1pNWH1LTWwApEs7QnQPTFDdBBiHLXA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-04 16:27 UTC (permalink / raw)
To: amd-gfx list, Christian König, Michel Dänzer
Hi,
I am a collaborator with Syncleus/aparapi project on github and I've
been testing OpenCL on AMD and NVIDIA cards.
Currently I have a set of kernels that hang the GPU (AMD RX 460 and
AMD RX 550) across all compute units on x86_64 running vanilla kernel
4.16.7 on Ubuntu 18.04, also on Ubuntu 16.04.4 with AMDGPU PRO 17.50
and 18.10 show the same problems, in fact, AMDGPU-PRO 18.10 is even
worse.
However the same set of kernels run happily on armhf with vanilla
Linux 4.16.7 and mesa 18.0 (mesa-opencl-icd and libclc for amdgcn),
Ubuntu 17.10, on an AMD RX460 and an AMD RX 550.
Luís Mendes
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1p3SnOnduP0nL1D1pNWH1LTWwApEs7QnQPTFDdBBiHLXA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-05-04 18:18 ` Abramov, Slava
[not found] ` <CY4PR12MB13045EA9BCBFAB20D698BA86FE860-rpdhrqHFk05fmUFYn07qFQdYzm3356FpvxpqHgZTriW3zl9H0oFU5g@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Abramov, Slava @ 2018-05-04 18:18 UTC (permalink / raw)
To: Luís Mendes, amd-gfx list, Koenig, Christian, Michel Dänzer
[-- Attachment #1.1: Type: text/plain, Size: 1307 bytes --]
Luis,
Can you please provide more details on your system environment and steps on configuring the software and reproducing the issue?
Slava A
________________________________
From: amd-gfx <amd-gfx-bounces-PD4FTy7X32lNgt0PjOBp9y5qC8QIuHrW@public.gmane.org> on behalf of Luís Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
Sent: Friday, May 4, 2018 12:27:47 PM
To: amd-gfx list; Koenig, Christian; Michel Dänzer
Subject: GPU hang trying to run OpenCL kernels on x86_64
Hi,
I am a collaborator with Syncleus/aparapi project on github and I've
been testing OpenCL on AMD and NVIDIA cards.
Currently I have a set of kernels that hang the GPU (AMD RX 460 and
AMD RX 550) across all compute units on x86_64 running vanilla kernel
4.16.7 on Ubuntu 18.04, also on Ubuntu 16.04.4 with AMDGPU PRO 17.50
and 18.10 show the same problems, in fact, AMDGPU-PRO 18.10 is even
worse.
However the same set of kernels run happily on armhf with vanilla
Linux 4.16.7 and mesa 18.0 (mesa-opencl-icd and libclc for amdgcn),
Ubuntu 17.10, on an AMD RX460 and an AMD RX 550.
Luís Mendes
_______________________________________________
amd-gfx mailing list
amd-gfx-PD4FTy7X32lNgt0PjOBp9y5qC8QIuHrW@public.gmane.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
[-- Attachment #1.2: Type: text/html, Size: 2435 bytes --]
[-- Attachment #2: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CY4PR12MB13045EA9BCBFAB20D698BA86FE860-rpdhrqHFk05fmUFYn07qFQdYzm3356FpvxpqHgZTriW3zl9H0oFU5g@public.gmane.org>
@ 2018-05-04 23:15 ` Luís Mendes
[not found] ` <CAEzXK1rJbXSpLUm=XQTLvySM4HJ45G9fQ0WCTPhnvdPETwUaYA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-04 23:15 UTC (permalink / raw)
To: Abramov, Slava; +Cc: Michel Dänzer, Koenig, Christian, amd-gfx list
[-- Attachment #1: Type: text/plain, Size: 3662 bytes --]
Hi Slava,
The two x86_64 systems I tried are:
- System One
Tyan S7025 with dual Xeon X5675 and 48GB registered ECC memory, with
a NVIDIA GTX 1050Ti 4GB(also used for display) and an AMD RX 550 4GB
Running standard Ubuntu 16.04.4 with kernels
linux-image-4.13.0-38-generic and linux-image-4.4.0-122-generic,
mesa-17.2.8-0ubuntu0, libdrm-2.4.83-1
and amdgpu-pro 17.50/amdgpu-pro 18.10
lsb_release -a
Description: Ubuntu 16.04.4 LTS
BIOS configuration:
ACPI enabled v3.0
ACPI APIC support Enabled
ACPI SRAT table Enabled
SR-IOV Enabled
Intel VT-d Disabled
PCI MMIO 64 Bits support Disabled
- System Two
Tyan S7002 with dual Xeon X5670 and 12GB registered ECC memory, with
an AMD RX 480
Running Ubuntu 18.04 with kernels vanilla 4.16.7 and
linux-image-4.15.0-20-generic, mesa-18.0.0~rc5-1ubuntu1,
libdrm-2.4.91-2
and mesa-opencl-icd, libclc-0.2.0+git20180312-1
BIOS configuration:
ACPI enabled v2.0
ACPI APIC support Enabled
ACPI SRAT table Enabled
SR-IOV Enabled
Intel VT-d Disabled
PCI MMIO 64 Bits support Disabled
amdgpu-pro-install --headless --opencl=legacy
When I try to run the attached openCL code (which computes a
cross-correlation between two square matrices directly by cross
correlation function definition), the GPU hangs, but there are also
other kernels where this also happens.
As soon as I try to run the kernel the system hangs at the first
kernel computation on all the two systems, and after a couple of
seconds dmesg shows:
[drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring gfx timeout, last
signaled seq=2, last emitted seq=3
[drm] IP block:gmc_v8_0 is hung!
[drm] IP block:tonga_ih is hung!
[drm] IP block:gfx_v8_0 is hung!
[drm] IP block:sdma_v3_0 is hung!
[drm] IP block:uvd_v6_0 is hung!
[drm] IP block:vce_v3_0 is hung!
[drm] GPU recovery disabled.
- On another system with armhf 32 bits, 1GB ram, 512GB SSD, AMD RX 480
or AMD RX 550
with Ubuntu 17.10, vanilla kernel 4.16.7, mesa-18.0.2,
libdrm-2.4.92-git, libclc-git at commit
3d994f2ff2cbb4531223fe2657144cb19f0c5328 (15/Nov/2017)
The kernels work properly on the same AMD cards.
On Fri, May 4, 2018 at 7:18 PM, Abramov, Slava <Slava.Abramov-5C7GfCeVMHo@public.gmane.org> wrote:
> Luis,
>
>
> Can you please provide more details on your system environment and steps on
> configuring the software and reproducing the issue?
>
>
>
> Slava A
>
> ________________________________
> From: amd-gfx <amd-gfx-bounces-PD4FTy7X32lNgt0PjOBp9y5qC8QIuHrW@public.gmane.org> on behalf of Luís
> Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
> Sent: Friday, May 4, 2018 12:27:47 PM
> To: amd-gfx list; Koenig, Christian; Michel Dänzer
> Subject: GPU hang trying to run OpenCL kernels on x86_64
>
> Hi,
>
> I am a collaborator with Syncleus/aparapi project on github and I've
> been testing OpenCL on AMD and NVIDIA cards.
>
> Currently I have a set of kernels that hang the GPU (AMD RX 460 and
> AMD RX 550) across all compute units on x86_64 running vanilla kernel
> 4.16.7 on Ubuntu 18.04, also on Ubuntu 16.04.4 with AMDGPU PRO 17.50
> and 18.10 show the same problems, in fact, AMDGPU-PRO 18.10 is even
> worse.
>
> However the same set of kernels run happily on armhf with vanilla
> Linux 4.16.7 and mesa 18.0 (mesa-opencl-icd and libclc for amdgcn),
> Ubuntu 17.10, on an AMD RX460 and an AMD RX 550.
>
> Luís Mendes
> _______________________________________________
> amd-gfx mailing list
> amd-gfx-PD4FTy7X32lNgt0PjOBp9y5qC8QIuHrW@public.gmane.org
> https://lists.freedesktop.org/mailman/listinfo/amd-gfx
[-- Attachment #2: kernel_xcorr.txt --]
[-- Type: text/plain, Size: 3930 bytes --]
May 04, 2018 10:37:41 PM com.aparapi.internal.kernel.KernelRunner executeInternalInner
INFO: typedef struct This_s{
__global int *tilesGeometry;
__global int *inputGeometry;
__global int *threadOutputStart;
__global int *outputGeometry;
__global int *threadOffsetI;
__global int *threadOffsetJ;
__global float *matrixInF;
__global float *matrixInG;
__global float *matrixOut;
int passid;
}This;
int get_pass_id(This *this){
return this->passid;
}
short pt_ist_ceris_vipivist_jobs_CrossCorrelationKernel__signX(This *this, short x){
short value = (short)((x + x) + 1);
return((short)(value / abs(value)));
}
short pt_ist_ceris_vipivist_jobs_CrossCorrelationKernel__relocateX(This *this, short x, short dimX){
short result = (short)(((pt_ist_ceris_vipivist_jobs_CrossCorrelationKernel__signX(this, x) + 1) * (x + 1)) / 2);
result = (short)(((pt_ist_ceris_vipivist_jobs_CrossCorrelationKernel__signX(this, (short)(dimX - result)) + 1) * result) / 2);
return(result);
}
__kernel void run(
__global int *tilesGeometry,
__global int *inputGeometry,
__global int *threadOutputStart,
__global int *outputGeometry,
__global int *threadOffsetI,
__global int *threadOffsetJ,
__global float *matrixInF,
__global float *matrixInG,
__global float *matrixOut,
int passid
){
This thisStruct;
This* this=&thisStruct;
this->tilesGeometry = tilesGeometry;
this->inputGeometry = inputGeometry;
this->threadOutputStart = threadOutputStart;
this->outputGeometry = outputGeometry;
this->threadOffsetI = threadOffsetI;
this->threadOffsetJ = threadOffsetJ;
this->matrixInF = matrixInF;
this->matrixInG = matrixInG;
this->matrixOut = matrixOut;
this->passid = passid;
{
int sizeI = get_global_size(1);
int sizeJ = get_global_size(0);
int i = get_global_id(1);
int j = get_global_id(0);
int k = get_global_id(2);
int il = get_local_id(0);
int jl = get_local_id(1);
int matrixInputStart = ((((k * this->tilesGeometry[0]) * this->tilesGeometry[1]) * (this->inputGeometry[1] + 1)) * (this->inputGeometry[0] + 1)) + (((this->threadOutputStart[((i * sizeJ) + j)] / (this->outputGeometry[0] * this->outputGeometry[1])) * (this->inputGeometry[0] + 1)) * (this->inputGeometry[1] + 1));
int matrixOutputStart = ((((k * this->tilesGeometry[0]) * this->tilesGeometry[1]) * this->outputGeometry[0]) * this->outputGeometry[1]) + this->threadOutputStart[((i * sizeJ) + j)];
short subMatrixI = (short)this->threadOffsetI[i];
short subMatrixJ = (short)this->threadOffsetJ[j];
float accum = 0.0f;
for (short indexN = (short)(-this->outputGeometry[0] / 2); indexN<=(this->outputGeometry[0] / 2); indexN = (short)(indexN + 1)){
for (short indexM = (short)(-this->outputGeometry[1] / 2); indexM<=(this->outputGeometry[1] / 2); indexM = (short)(indexM + 1)){
short fi = pt_ist_ceris_vipivist_jobs_CrossCorrelationKernel__relocateX(this, indexN, (short)this->inputGeometry[0]);
short fj = pt_ist_ceris_vipivist_jobs_CrossCorrelationKernel__relocateX(this, indexM, (short)this->inputGeometry[1]);
short gi = pt_ist_ceris_vipivist_jobs_CrossCorrelationKernel__relocateX(this, (short)(subMatrixI + indexN), (short)this->inputGeometry[0]);
short gj = pt_ist_ceris_vipivist_jobs_CrossCorrelationKernel__relocateX(this, (short)(subMatrixJ + indexM), (short)this->inputGeometry[1]);
accum = accum + (this->matrixInF[((matrixInputStart + (fi * (this->inputGeometry[1] + 1))) + fj)] * this->matrixInG[((matrixInputStart + (gi * (this->inputGeometry[1] + 1))) + gj)]);
}
}
int outIndex = (matrixOutputStart + ((subMatrixI + (this->outputGeometry[0] / 2)) * this->outputGeometry[1])) + (subMatrixJ + (this->outputGeometry[1] / 2));
this->matrixOut[outIndex] = accum;
return;
}
}
[-- Attachment #3: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1rJbXSpLUm=XQTLvySM4HJ45G9fQ0WCTPhnvdPETwUaYA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-05-07 9:38 ` Michel Dänzer
[not found] ` <53cc38f2-e94a-1514-0a03-303101db2f88-otUistvHUpPR7s880joybQ@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Michel Dänzer @ 2018-05-07 9:38 UTC (permalink / raw)
To: Luís Mendes, Abramov, Slava; +Cc: Koenig, Christian, amd-gfx list
On 2018-05-05 01:15 AM, Luís Mendes wrote:
>
> - On another system with armhf 32 bits, 1GB ram, 512GB SSD, AMD RX 480
> or AMD RX 550
> with Ubuntu 17.10, vanilla kernel 4.16.7, mesa-18.0.2,
> libdrm-2.4.92-git, libclc-git at commit
> 3d994f2ff2cbb4531223fe2657144cb19f0c5328 (15/Nov/2017)
>
> The kernels work properly on the same AMD cards.
Have you tried those exact same versions of the kernel, Mesa, libclc and
LLVM on x86?
--
Earthling Michel Dänzer | http://www.amd.com
Libre software enthusiast | Mesa and X developer
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <53cc38f2-e94a-1514-0a03-303101db2f88-otUistvHUpPR7s880joybQ@public.gmane.org>
@ 2018-05-07 12:31 ` Luís Mendes
[not found] ` <CAEzXK1qHtfOBgismLvNy_x+NcMw78288AuwovBR-JmRwqpDmGQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-07 12:31 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
Hi Michel,
No, I haven't tried the exact same versions of Mesa, nor libclc, nor
LLVM on x86, however on armhf I have been able to use several
combinations of Linux kernel versions and mesa versions which are able
to run the OpenCL kernels in question. I will try to see if the same
happens with the exact same Ubuntu 18.04 LTS base installation on
armhf, but won't be able to test it today.
Luís
On Mon, May 7, 2018 at 10:38 AM, Michel Dänzer <michel@daenzer.net> wrote:
> On 2018-05-05 01:15 AM, Luís Mendes wrote:
>>
>> - On another system with armhf 32 bits, 1GB ram, 512GB SSD, AMD RX 480
>> or AMD RX 550
>> with Ubuntu 17.10, vanilla kernel 4.16.7, mesa-18.0.2,
>> libdrm-2.4.92-git, libclc-git at commit
>> 3d994f2ff2cbb4531223fe2657144cb19f0c5328 (15/Nov/2017)
>>
>> The kernels work properly on the same AMD cards.
>
> Have you tried those exact same versions of the kernel, Mesa, libclc and
> LLVM on x86?
>
>
> --
> Earthling Michel Dänzer | http://www.amd.com
> Libre software enthusiast | Mesa and X developer
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1qHtfOBgismLvNy_x+NcMw78288AuwovBR-JmRwqpDmGQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-05-11 12:15 ` Luís Mendes
[not found] ` <CAEzXK1oM6b1bV3R3ezwD4eYrJXWV9+cdUFMC4q5+1bPkpmJFqQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-11 12:15 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
Hi Michel,
Just made a fresh Ubuntu 18.04 LTS install for armhf with ubuntu
default mesa, libdrm and libclc, with the same 4.16.7 kernel and it
runs fine with the OpenCL applications that cause the hang on x86_64.
So it is surely a kernel or mesa issue exclusive to x86_64, libraries
versions are the same on both systems now, as well as the kernel.
I have even tried amdgpu-pro-18.20 with ubuntu 18.04 on x86_64 and it
hangs just the same.
Regards,
Luís
On Mon, May 7, 2018 at 1:31 PM, Luís Mendes <luis.p.mendes@gmail.com> wrote:
> Hi Michel,
>
> No, I haven't tried the exact same versions of Mesa, nor libclc, nor
> LLVM on x86, however on armhf I have been able to use several
> combinations of Linux kernel versions and mesa versions which are able
> to run the OpenCL kernels in question. I will try to see if the same
> happens with the exact same Ubuntu 18.04 LTS base installation on
> armhf, but won't be able to test it today.
>
> Luís
>
> On Mon, May 7, 2018 at 10:38 AM, Michel Dänzer <michel@daenzer.net> wrote:
>> On 2018-05-05 01:15 AM, Luís Mendes wrote:
>>>
>>> - On another system with armhf 32 bits, 1GB ram, 512GB SSD, AMD RX 480
>>> or AMD RX 550
>>> with Ubuntu 17.10, vanilla kernel 4.16.7, mesa-18.0.2,
>>> libdrm-2.4.92-git, libclc-git at commit
>>> 3d994f2ff2cbb4531223fe2657144cb19f0c5328 (15/Nov/2017)
>>>
>>> The kernels work properly on the same AMD cards.
>>
>> Have you tried those exact same versions of the kernel, Mesa, libclc and
>> LLVM on x86?
>>
>>
>> --
>> Earthling Michel Dänzer | http://www.amd.com
>> Libre software enthusiast | Mesa and X developer
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1oM6b1bV3R3ezwD4eYrJXWV9+cdUFMC4q5+1bPkpmJFqQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-05-23 22:06 ` Luís Mendes
[not found] ` <CAEzXK1qRWkL67rG40jk4Odqm8AjbDvnnaCsDycLPRcPXXPL-KQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-23 22:06 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
[-- Attachment #1.1: Type: text/plain, Size: 2550 bytes --]
I've tried Linux 4.17-rc6 with Ubuntu 18.04 on Tyan S7002 and I am not even
able see lightdm/gdm3 as system hangs when starting X.
Having SR-IOV enabled or disabled makes no difference.
Tested with AMD RX 460.
When X is supposed to start the system hangs and only a rectangular region
on the top left corner screen remains with console text messages from the
boot process while the remaining of the screen is just black. I am unable
to do anything with the keyboard, switching to console does not work,
ctrl-alt-del also doesn't work. I've to do a cold reset.
Regards,
Luís
On Fri, May 11, 2018 at 1:15 PM, Luís Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
wrote:
> Hi Michel,
>
> Just made a fresh Ubuntu 18.04 LTS install for armhf with ubuntu
> default mesa, libdrm and libclc, with the same 4.16.7 kernel and it
> runs fine with the OpenCL applications that cause the hang on x86_64.
> So it is surely a kernel or mesa issue exclusive to x86_64, libraries
> versions are the same on both systems now, as well as the kernel.
> I have even tried amdgpu-pro-18.20 with ubuntu 18.04 on x86_64 and it
> hangs just the same.
>
> Regards,
> Luís
>
> On Mon, May 7, 2018 at 1:31 PM, Luís Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
> wrote:
> > Hi Michel,
> >
> > No, I haven't tried the exact same versions of Mesa, nor libclc, nor
> > LLVM on x86, however on armhf I have been able to use several
> > combinations of Linux kernel versions and mesa versions which are able
> > to run the OpenCL kernels in question. I will try to see if the same
> > happens with the exact same Ubuntu 18.04 LTS base installation on
> > armhf, but won't be able to test it today.
> >
> > Luís
> >
> > On Mon, May 7, 2018 at 10:38 AM, Michel Dänzer <michel-otUistvHUpPR7s880joybQ@public.gmane.org>
> wrote:
> >> On 2018-05-05 01:15 AM, Luís Mendes wrote:
> >>>
> >>> - On another system with armhf 32 bits, 1GB ram, 512GB SSD, AMD RX 480
> >>> or AMD RX 550
> >>> with Ubuntu 17.10, vanilla kernel 4.16.7, mesa-18.0.2,
> >>> libdrm-2.4.92-git, libclc-git at commit
> >>> 3d994f2ff2cbb4531223fe2657144cb19f0c5328 (15/Nov/2017)
> >>>
> >>> The kernels work properly on the same AMD cards.
> >>
> >> Have you tried those exact same versions of the kernel, Mesa, libclc and
> >> LLVM on x86?
> >>
> >>
> >> --
> >> Earthling Michel Dänzer |
> http://www.amd.com
> >> Libre software enthusiast | Mesa and X developer
>
[-- Attachment #1.2: Type: text/html, Size: 3528 bytes --]
[-- Attachment #2: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1qRWkL67rG40jk4Odqm8AjbDvnnaCsDycLPRcPXXPL-KQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-05-24 8:30 ` Michel Dänzer
[not found] ` <22178876-688c-b4fe-d40e-1bab28024603-otUistvHUpPR7s880joybQ@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Michel Dänzer @ 2018-05-24 8:30 UTC (permalink / raw)
To: Luís Mendes; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
On 2018-05-24 12:06 AM, Luís Mendes wrote:
> I've tried Linux 4.17-rc6 with Ubuntu 18.04 on Tyan S7002 and I am not even
> able see lightdm/gdm3 as system hangs when starting X.
> Having SR-IOV enabled or disabled makes no difference.
> Tested with AMD RX 460.
> When X is supposed to start the system hangs and only a rectangular region
> on the top left corner screen remains with console text messages from the
> boot process while the remaining of the screen is just black. I am unable
> to do anything with the keyboard, switching to console does not work,
> ctrl-alt-del also doesn't work. I've to do a cold reset.
Can you isolate which change introduced this new issue with git bisect?
--
Earthling Michel Dänzer | http://www.amd.com
Libre software enthusiast | Mesa and X developer
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <22178876-688c-b4fe-d40e-1bab28024603-otUistvHUpPR7s880joybQ@public.gmane.org>
@ 2018-05-24 8:55 ` Luís Mendes
[not found] ` <CAEzXK1q+pMZgg7a7TMkNaDPhe90NkCc7MtAfE98vRY5tGDfW4A-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-24 8:55 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
[-- Attachment #1.1: Type: text/plain, Size: 1356 bytes --]
Hi Michel,
I will have to check previous rc releases of 4.17 to see if it wasn't
already happening, before trying any possible git bisect.
As an update I can say that an AMD Radeon R7 240 works fine on the same
system with the same kernel and I am able to run the OpenCL kernels, that I
couldn't with RX 460/RX 550.
Regards,
Luís
On Thu, May 24, 2018 at 9:30 AM, Michel Dänzer <michel-otUistvHUpPR7s880joybQ@public.gmane.org> wrote:
> On 2018-05-24 12:06 AM, Luís Mendes wrote:
> > I've tried Linux 4.17-rc6 with Ubuntu 18.04 on Tyan S7002 and I am not
> even
> > able see lightdm/gdm3 as system hangs when starting X.
> > Having SR-IOV enabled or disabled makes no difference.
> > Tested with AMD RX 460.
> > When X is supposed to start the system hangs and only a rectangular
> region
> > on the top left corner screen remains with console text messages from the
> > boot process while the remaining of the screen is just black. I am unable
> > to do anything with the keyboard, switching to console does not work,
> > ctrl-alt-del also doesn't work. I've to do a cold reset.
>
> Can you isolate which change introduced this new issue with git bisect?
>
>
> --
> Earthling Michel Dänzer | http://www.amd.com
> Libre software enthusiast | Mesa and X developer
>
[-- Attachment #1.2: Type: text/html, Size: 1989 bytes --]
[-- Attachment #2: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1q+pMZgg7a7TMkNaDPhe90NkCc7MtAfE98vRY5tGDfW4A-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-05-24 9:01 ` Luís Mendes
[not found] ` <CAEzXK1pZqFMZ8Qos3h7E-aYdmBE18GKFSamPV+0ZsXu=CatKRA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-24 9:01 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
[-- Attachment #1.1: Type: text/plain, Size: 1902 bytes --]
Hi Michel,
So summarizing with Linux kernel 4.17-rc6 on Ubuntu 18.04 using AMD RX
460/RX 550 I am not able to enter X.
The same system with AMD Radeon R7 240 not only enters X as also runs the
OpenCL kernel that RX 460 / RX 550 are unable to run for all the kernels
that I have tested.
Could this also be a Mesa issue, regarding OpenCL on RX 460?
Regards,
Luís
On Thu, May 24, 2018 at 9:55 AM, Luís Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
wrote:
> Hi Michel,
>
> I will have to check previous rc releases of 4.17 to see if it wasn't
> already happening, before trying any possible git bisect.
> As an update I can say that an AMD Radeon R7 240 works fine on the same
> system with the same kernel and I am able to run the OpenCL kernels, that I
> couldn't with RX 460/RX 550.
>
> Regards,
> Luís
>
> On Thu, May 24, 2018 at 9:30 AM, Michel Dänzer <michel-otUistvHUpPR7s880joybQ@public.gmane.org> wrote:
>
>> On 2018-05-24 12:06 AM, Luís Mendes wrote:
>> > I've tried Linux 4.17-rc6 with Ubuntu 18.04 on Tyan S7002 and I am not
>> even
>> > able see lightdm/gdm3 as system hangs when starting X.
>> > Having SR-IOV enabled or disabled makes no difference.
>> > Tested with AMD RX 460.
>> > When X is supposed to start the system hangs and only a rectangular
>> region
>> > on the top left corner screen remains with console text messages from
>> the
>> > boot process while the remaining of the screen is just black. I am
>> unable
>> > to do anything with the keyboard, switching to console does not work,
>> > ctrl-alt-del also doesn't work. I've to do a cold reset.
>>
>> Can you isolate which change introduced this new issue with git bisect?
>>
>>
>> --
>> Earthling Michel Dänzer | http://www.amd.com
>> Libre software enthusiast | Mesa and X developer
>>
>
>
[-- Attachment #1.2: Type: text/html, Size: 2968 bytes --]
[-- Attachment #2: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1pZqFMZ8Qos3h7E-aYdmBE18GKFSamPV+0ZsXu=CatKRA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-05-24 9:13 ` Luís Mendes
[not found] ` <CAEzXK1qtjy+OaBh5rkzOXrTYe4Zq1w5bzdzTSRuCuDcm-kx-fA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-24 9:13 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
[-- Attachment #1.1: Type: text/plain, Size: 2457 bytes --]
Hi Michel,
I also work as a researcher at a university and we are considering buying
AMD cards to do OpenCL computations for numerical modelling, but currently
I am unable to give a try at the AMD cards I have at home.
I couldn't find any working driver for them... also amdgpu-pro drivers
don't work, or at least I have been unable to make them work.
Regards,
Luís
On Thu, May 24, 2018 at 10:01 AM, Luís Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
wrote:
> Hi Michel,
>
> So summarizing with Linux kernel 4.17-rc6 on Ubuntu 18.04 using AMD RX
> 460/RX 550 I am not able to enter X.
> The same system with AMD Radeon R7 240 not only enters X as also runs the
> OpenCL kernel that RX 460 / RX 550 are unable to run for all the kernels
> that I have tested.
> Could this also be a Mesa issue, regarding OpenCL on RX 460?
>
> Regards,
> Luís
>
> On Thu, May 24, 2018 at 9:55 AM, Luís Mendes <luis.p.mendes-Re5JQEeQqe8@public.gmane.orgm>
> wrote:
>
>> Hi Michel,
>>
>> I will have to check previous rc releases of 4.17 to see if it wasn't
>> already happening, before trying any possible git bisect.
>> As an update I can say that an AMD Radeon R7 240 works fine on the same
>> system with the same kernel and I am able to run the OpenCL kernels, that I
>> couldn't with RX 460/RX 550.
>>
>> Regards,
>> Luís
>>
>> On Thu, May 24, 2018 at 9:30 AM, Michel Dänzer <michel-otUistvHUpPR7s880joybQ@public.gmane.org>
>> wrote:
>>
>>> On 2018-05-24 12:06 AM, Luís Mendes wrote:
>>> > I've tried Linux 4.17-rc6 with Ubuntu 18.04 on Tyan S7002 and I am not
>>> even
>>> > able see lightdm/gdm3 as system hangs when starting X.
>>> > Having SR-IOV enabled or disabled makes no difference.
>>> > Tested with AMD RX 460.
>>> > When X is supposed to start the system hangs and only a rectangular
>>> region
>>> > on the top left corner screen remains with console text messages from
>>> the
>>> > boot process while the remaining of the screen is just black. I am
>>> unable
>>> > to do anything with the keyboard, switching to console does not work,
>>> > ctrl-alt-del also doesn't work. I've to do a cold reset.
>>>
>>> Can you isolate which change introduced this new issue with git bisect?
>>>
>>>
>>> --
>>> Earthling Michel Dänzer | http://www.amd.com
>>> Libre software enthusiast | Mesa and X developer
>>>
>>
>>
>
[-- Attachment #1.2: Type: text/html, Size: 3951 bytes --]
[-- Attachment #2: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1qtjy+OaBh5rkzOXrTYe4Zq1w5bzdzTSRuCuDcm-kx-fA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-05-24 10:18 ` Luís Mendes
[not found] ` <CAEzXK1ryiqqrxTr5mn+Y4VvNAn-LtQb-0cBTitKKoQb+4B1=Qg-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-24 10:18 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
[-- Attachment #1.1: Type: text/plain, Size: 3247 bytes --]
Additional update...
I was able to boot and enter X by installing an NVIDIA GTX 1050 Ti as the
primary display card and using an AMD RX 550 as the secondary card on the
Tyan S7025 with the same Ubuntu 18.04 and the same Linux kernel 4.17-rc6.
However once I try to run an OpenCL kernel on RX 550 I get a sdma1 timeout
and the GPU hangs, which likely what is happening when I boot with RX 550
as the single GPU card on the system.
This means it is not an issue introduced in 4.17-rc6, it just means that I
didn't notice the effect of the system with the two GPUs vs system with
single AMD GPU.
The dmesg log follows attached.
Luís
On Thu, May 24, 2018 at 10:13 AM, Luís Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
wrote:
> Hi Michel,
>
> I also work as a researcher at a university and we are considering buying
> AMD cards to do OpenCL computations for numerical modelling, but currently
> I am unable to give a try at the AMD cards I have at home.
> I couldn't find any working driver for them... also amdgpu-pro drivers
> don't work, or at least I have been unable to make them work.
>
> Regards,
> Luís
>
> On Thu, May 24, 2018 at 10:01 AM, Luís Mendes <luis.p.mendes@gmail.com>
> wrote:
>
>> Hi Michel,
>>
>> So summarizing with Linux kernel 4.17-rc6 on Ubuntu 18.04 using AMD RX
>> 460/RX 550 I am not able to enter X.
>> The same system with AMD Radeon R7 240 not only enters X as also runs the
>> OpenCL kernel that RX 460 / RX 550 are unable to run for all the kernels
>> that I have tested.
>> Could this also be a Mesa issue, regarding OpenCL on RX 460?
>>
>> Regards,
>> Luís
>>
>> On Thu, May 24, 2018 at 9:55 AM, Luís Mendes <luis.p.mendes@gmail.com>
>> wrote:
>>
>>> Hi Michel,
>>>
>>> I will have to check previous rc releases of 4.17 to see if it wasn't
>>> already happening, before trying any possible git bisect.
>>> As an update I can say that an AMD Radeon R7 240 works fine on the same
>>> system with the same kernel and I am able to run the OpenCL kernels, that I
>>> couldn't with RX 460/RX 550.
>>>
>>> Regards,
>>> Luís
>>>
>>> On Thu, May 24, 2018 at 9:30 AM, Michel Dänzer <michel-otUistvHUpPR7s880joybQ@public.gmane.org>
>>> wrote:
>>>
>>>> On 2018-05-24 12:06 AM, Luís Mendes wrote:
>>>> > I've tried Linux 4.17-rc6 with Ubuntu 18.04 on Tyan S7002 and I am
>>>> not even
>>>> > able see lightdm/gdm3 as system hangs when starting X.
>>>> > Having SR-IOV enabled or disabled makes no difference.
>>>> > Tested with AMD RX 460.
>>>> > When X is supposed to start the system hangs and only a rectangular
>>>> region
>>>> > on the top left corner screen remains with console text messages from
>>>> the
>>>> > boot process while the remaining of the screen is just black. I am
>>>> unable
>>>> > to do anything with the keyboard, switching to console does not work,
>>>> > ctrl-alt-del also doesn't work. I've to do a cold reset.
>>>>
>>>> Can you isolate which change introduced this new issue with git bisect?
>>>>
>>>>
>>>> --
>>>> Earthling Michel Dänzer |
>>>> http://www.amd.com
>>>> Libre software enthusiast | Mesa and X developer
>>>>
>>>
>>>
>>
>
[-- Attachment #1.2: Type: text/html, Size: 5363 bytes --]
[-- Attachment #2: amdgpu_logs1.txt --]
[-- Type: text/plain, Size: 84957 bytes --]
[ 0.000000] KERNEL supported cpus:
[ 0.000000] Intel GenuineIntel
[ 0.000000] AMD AuthenticAMD
[ 0.000000] Centaur CentaurHauls
[ 0.000000] x86/fpu: x87 FPU will use FXSAVE
[ 0.000000] e820: BIOS-provided physical RAM map:
[ 0.000000] BIOS-e820: [mem 0x0000000000000000-0x000000000009d3ff] usable
[ 0.000000] BIOS-e820: [mem 0x000000000009d400-0x000000000009ffff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000000e0000-0x00000000000fffff] reserved
[ 0.000000] BIOS-e820: [mem 0x0000000000100000-0x00000000bf76ffff] usable
[ 0.000000] BIOS-e820: [mem 0x00000000bf770000-0x00000000bf77dfff] ACPI data
[ 0.000000] BIOS-e820: [mem 0x00000000bf77e000-0x00000000bf7cffff] ACPI NVS
[ 0.000000] BIOS-e820: [mem 0x00000000bf7d0000-0x00000000bf7dffff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000bf7ec000-0x00000000bfffffff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000e0000000-0x00000000efffffff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000fee00000-0x00000000fee00fff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000ffa00000-0x00000000ffffffff] reserved
[ 0.000000] BIOS-e820: [mem 0x0000000100000000-0x0000000c3fffffff] usable
[ 0.000000] NX (Execute Disable) protection: active
[ 0.000000] SMBIOS 2.6 present.
[ 0.000000] DMI: TYAN empty/S7025, BIOS 'V1.09A' 06/19/2012
[ 0.000000] e820: update [mem 0x00000000-0x00000fff] usable ==> reserved
[ 0.000000] e820: remove [mem 0x000a0000-0x000fffff] usable
[ 0.000000] e820: last_pfn = 0xc40000 max_arch_pfn = 0x400000000
[ 0.000000] MTRR default type: uncachable
[ 0.000000] MTRR fixed ranges enabled:
[ 0.000000] 00000-9FFFF write-back
[ 0.000000] A0000-BFFFF uncachable
[ 0.000000] C0000-CFFFF write-protect
[ 0.000000] D0000-DFFFF uncachable
[ 0.000000] E0000-E3FFF write-protect
[ 0.000000] E4000-EFFFF write-through
[ 0.000000] F0000-FFFFF write-protect
[ 0.000000] MTRR variable ranges enabled:
[ 0.000000] 0 base 0000000000 mask F800000000 write-back
[ 0.000000] 1 base 0800000000 mask FC00000000 write-back
[ 0.000000] 2 base 0C00000000 mask FFC0000000 write-back
[ 0.000000] 3 base 00C0000000 mask FFC0000000 uncachable
[ 0.000000] 4 base 00BF800000 mask FFFF800000 uncachable
[ 0.000000] 5 disabled
[ 0.000000] 6 disabled
[ 0.000000] 7 disabled
[ 0.000000] 8 disabled
[ 0.000000] 9 disabled
[ 0.000000] x86/PAT: Configuration [0-7]: WB WC UC- UC WB WP UC- WT
[ 0.000000] total RAM covered: 49144M
[ 0.000000] Found optimal setting for mtrr clean up
[ 0.000000] gran_size: 64K chunk_size: 16M num_reg: 8 lose cover RAM: 0G
[ 0.000000] e820: update [mem 0xbf800000-0xffffffff] usable ==> reserved
[ 0.000000] e820: last_pfn = 0xbf770 max_arch_pfn = 0x400000000
[ 0.000000] found SMP MP-table at [mem 0x000ff780-0x000ff78f] mapped at [ (ptrval)]
[ 0.000000] Scanning 1 areas for low memory corruption
[ 0.000000] Base memory trampoline at [ (ptrval)] 97000 size 24576
[ 0.000000] Using GB pages for direct mapping
[ 0.000000] BRK [0x62b949000, 0x62b949fff] PGTABLE
[ 0.000000] BRK [0x62b94a000, 0x62b94afff] PGTABLE
[ 0.000000] BRK [0x62b94b000, 0x62b94bfff] PGTABLE
[ 0.000000] BRK [0x62b94c000, 0x62b94cfff] PGTABLE
[ 0.000000] BRK [0x62b94d000, 0x62b94dfff] PGTABLE
[ 0.000000] BRK [0x62b94e000, 0x62b94efff] PGTABLE
[ 0.000000] RAMDISK: [mem 0x31e3f000-0x34f16fff]
[ 0.000000] ACPI: Early table checksum verification disabled
[ 0.000000] ACPI: RSDP 0x00000000000FADD0 000024 (v02 ACPIAM)
[ 0.000000] ACPI: XSDT 0x00000000BF770100 00005C (v01 061912 XSDT1941 20120619 MSFT 00000097)
[ 0.000000] ACPI: FACP 0x00000000BF770290 0000F4 (v04 061912 FACP1941 20120619 MSFT 00000097)
[ 0.000000] ACPI BIOS Warning (bug): 32/64X length mismatch in FADT/Gpe0Block: 128/64 (20180313/tbfadt-569)
[ 0.000000] ACPI: DSDT 0x00000000BF770500 00725F (v02 7025_ 7025_001 00000001 INTL 20051117)
[ 0.000000] ACPI: FACS 0x00000000BF77E000 000040
[ 0.000000] ACPI: FACS 0x00000000BF77E000 000040
[ 0.000000] ACPI: APIC 0x00000000BF770390 00012A (v02 061912 APIC1941 20120619 MSFT 00000097)
[ 0.000000] ACPI: MCFG 0x00000000BF7704C0 00003C (v01 061912 OEMMCFG 20120619 MSFT 00000097)
[ 0.000000] ACPI: OEMB 0x00000000BF77E040 0000C0 (v01 061912 OEMB1941 20120619 MSFT 00000097)
[ 0.000000] ACPI: HPET 0x00000000BF77A500 000038 (v01 061912 OEMHPET 20120619 MSFT 00000097)
[ 0.000000] ACPI: SRAT 0x00000000BF77A540 000250 (v02 061912 OEMSRAT 00000001 INTL 00000001)
[ 0.000000] ACPI: SSDT 0x00000000BF785400 000363 (v01 DpgPmm CpuPm 00000012 INTL 20051117)
[ 0.000000] ACPI: Local APIC address 0xfee00000
[ 0.000000] SRAT: PXM 0 -> APIC 0x00 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x02 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x04 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x10 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x12 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x14 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x01 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x03 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x05 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x11 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x13 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x15 -> Node 0
[ 0.000000] SRAT: PXM 1 -> APIC 0x20 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x22 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x24 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x30 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x32 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x34 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x21 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x23 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x25 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x31 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x33 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x35 -> Node 1
[ 0.000000] ACPI: SRAT: Node 0 PXM 0 [mem 0x00000000-0x0009ffff]
[ 0.000000] ACPI: SRAT: Node 0 PXM 0 [mem 0x00100000-0xbfffffff]
[ 0.000000] ACPI: SRAT: Node 0 PXM 0 [mem 0x100000000-0x63fffffff]
[ 0.000000] ACPI: SRAT: Node 1 PXM 1 [mem 0x640000000-0xc3fffffff]
[ 0.000000] NUMA: Node 0 [mem 0x00000000-0x0009ffff] + [mem 0x00100000-0xbfffffff] -> [mem 0x00000000-0xbfffffff]
[ 0.000000] NUMA: Node 0 [mem 0x00000000-0xbfffffff] + [mem 0x100000000-0x63fffffff] -> [mem 0x00000000-0x63fffffff]
[ 0.000000] NODE_DATA(0) allocated [mem 0x63ffd5000-0x63fffffff]
[ 0.000000] NODE_DATA(1) allocated [mem 0xc3ffd5000-0xc3fffffff]
[ 0.000000] tsc: Fast TSC calibration using PIT
[ 0.000000] Zone ranges:
[ 0.000000] DMA [mem 0x0000000000001000-0x0000000000ffffff]
[ 0.000000] DMA32 [mem 0x0000000001000000-0x00000000ffffffff]
[ 0.000000] Normal [mem 0x0000000100000000-0x0000000c3fffffff]
[ 0.000000] Device empty
[ 0.000000] Movable zone start for each node
[ 0.000000] Early memory node ranges
[ 0.000000] node 0: [mem 0x0000000000001000-0x000000000009cfff]
[ 0.000000] node 0: [mem 0x0000000000100000-0x00000000bf76ffff]
[ 0.000000] node 0: [mem 0x0000000100000000-0x000000063fffffff]
[ 0.000000] node 1: [mem 0x0000000640000000-0x0000000c3fffffff]
[ 0.000000] Initmem setup node 0 [mem 0x0000000000001000-0x000000063fffffff]
[ 0.000000] On node 0 totalpages: 6289164
[ 0.000000] DMA zone: 64 pages used for memmap
[ 0.000000] DMA zone: 21 pages reserved
[ 0.000000] DMA zone: 3996 pages, LIFO batch:0
[ 0.000000] DMA32 zone: 12190 pages used for memmap
[ 0.000000] DMA32 zone: 780144 pages, LIFO batch:31
[ 0.000000] Normal zone: 86016 pages used for memmap
[ 0.000000] Normal zone: 5505024 pages, LIFO batch:31
[ 0.000000] Initmem setup node 1 [mem 0x0000000640000000-0x0000000c3fffffff]
[ 0.000000] On node 1 totalpages: 6291456
[ 0.000000] Normal zone: 98304 pages used for memmap
[ 0.000000] Normal zone: 6291456 pages, LIFO batch:31
[ 0.000000] Reserved but unavailable: 100 pages
[ 0.000000] ACPI: PM-Timer IO Port: 0x808
[ 0.000000] ACPI: Local APIC address 0xfee00000
[ 0.000000] ACPI: LAPIC_NMI (acpi_id[0xff] high dfl lint[0x1])
[ 0.000000] IOAPIC[0]: apic_id 6, version 32, address 0xfec00000, GSI 0-23
[ 0.000000] IOAPIC[1]: apic_id 7, version 32, address 0xfec8a000, GSI 24-47
[ 0.000000] IOAPIC[2]: apic_id 8, version 32, address 0xfec9a000, GSI 48-71
[ 0.000000] ACPI: INT_SRC_OVR (bus 0 bus_irq 0 global_irq 2 dfl dfl)
[ 0.000000] ACPI: INT_SRC_OVR (bus 0 bus_irq 9 global_irq 9 high level)
[ 0.000000] ACPI: IRQ0 used by override.
[ 0.000000] ACPI: IRQ9 used by override.
[ 0.000000] Using ACPI (MADT) for SMP configuration information
[ 0.000000] ACPI: HPET id: 0x8086a301 base: 0xfed00000
[ 0.000000] smpboot: Allowing 24 CPUs, 0 hotplug CPUs
[ 0.000000] PM: Registered nosave memory: [mem 0x00000000-0x00000fff]
[ 0.000000] PM: Registered nosave memory: [mem 0x0009d000-0x0009dfff]
[ 0.000000] PM: Registered nosave memory: [mem 0x0009e000-0x0009ffff]
[ 0.000000] PM: Registered nosave memory: [mem 0x000a0000-0x000dffff]
[ 0.000000] PM: Registered nosave memory: [mem 0x000e0000-0x000fffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf770000-0xbf77dfff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf77e000-0xbf7cffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf7d0000-0xbf7dffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf7e0000-0xbf7ebfff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf7ec000-0xbfffffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xc0000000-0xdfffffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xe0000000-0xefffffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xf0000000-0xfedfffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xfee00000-0xfee00fff]
[ 0.000000] PM: Registered nosave memory: [mem 0xfee01000-0xff9fffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xffa00000-0xffffffff]
[ 0.000000] e820: [mem 0xc0000000-0xdfffffff] available for PCI devices
[ 0.000000] Booting paravirtualized kernel on bare hardware
[ 0.000000] clocksource: refined-jiffies: mask: 0xffffffff max_cycles: 0xffffffff, max_idle_ns: 7645519600211568 ns
[ 0.000000] random: get_random_bytes called from start_kernel+0x99/0x55a with crng_init=0
[ 0.000000] setup_percpu: NR_CPUS:8192 nr_cpumask_bits:24 nr_cpu_ids:24 nr_node_ids:2
[ 0.000000] percpu: Embedded 46 pages/cpu @ (ptrval) s151552 r8192 d28672 u262144
[ 0.000000] pcpu-alloc: s151552 r8192 d28672 u262144 alloc=1*2097152
[ 0.000000] pcpu-alloc: [0] 00 01 02 03 04 05 12 13 [0] 14 15 16 17 -- -- -- --
[ 0.000000] pcpu-alloc: [1] 06 07 08 09 10 11 18 19 [1] 20 21 22 23 -- -- -- --
[ 0.000000] Built 2 zonelists, mobility grouping on. Total pages: 12384025
[ 0.000000] Policy zone: Normal
[ 0.000000] Kernel command line: BOOT_IMAGE=/boot/vmlinuz-4.17.0-rc6 root=UUID=1fd09015-7f74-4838-bbbd-00bb887c940f ro quiet splash vt.handoff=1
[ 0.000000] Calgary: detecting Calgary via BIOS EBDA area
[ 0.000000] Calgary: Unable to locate Rio Grande table in EBDA - bailing!
[ 0.000000] Memory: 49387164K/50322480K available (12300K kernel code, 2520K rwdata, 4332K rodata, 2428K init, 2384K bss, 935316K reserved, 0K cma-reserved)
[ 0.000000] SLUB: HWalign=64, Order=0-3, MinObjects=0, CPUs=24, Nodes=2
[ 0.000000] Kernel/User page tables isolation: enabled
[ 0.000000] ftrace: allocating 40314 entries in 158 pages
[ 0.000000] Hierarchical RCU implementation.
[ 0.000000] RCU restricting CPUs from NR_CPUS=8192 to nr_cpu_ids=24.
[ 0.000000] Tasks RCU enabled.
[ 0.000000] RCU: Adjusting geometry for rcu_fanout_leaf=16, nr_cpu_ids=24
[ 0.000000] NR_IRQS: 524544, nr_irqs: 1432, preallocated irqs: 16
[ 0.000000] Console: colour dummy device 80x25
[ 0.000000] console [tty0] enabled
[ 0.000000] mempolicy: Enabling automatic NUMA balancing. Configure with numa_balancing= or the kernel.numa_balancing sysctl
[ 0.000000] ACPI: Core revision 20180313
[ 0.000000] clocksource: hpet: mask: 0xffffffff max_cycles: 0xffffffff, max_idle_ns: 133484882848 ns
[ 0.000000] hpet clockevent registered
[ 0.000000] APIC: Switch to symmetric I/O mode setup
[ 0.000000] Switched APIC routing to physical flat.
[ 0.000000] ..TIMER: vector=0x30 apic1=0 pin1=2 apic2=-1 pin2=-1
[ 0.020000] tsc: Fast TSC calibration using PIT
[ 0.024000] tsc: Detected 3066.747 MHz processor
[ 0.024000] clocksource: tsc-early: mask: 0xffffffffffffffff max_cycles: 0x2c3492efe00, max_idle_ns: 440795313049 ns
[ 0.024000] Calibrating delay loop (skipped), value calculated using timer frequency.. 6133.49 BogoMIPS (lpj=12266988)
[ 0.024000] pid_max: default: 32768 minimum: 301
[ 0.024000] Security Framework initialized
[ 0.024000] Yama: becoming mindful.
[ 0.024000] AppArmor: AppArmor initialized
[ 0.039483] Dentry cache hash table entries: 8388608 (order: 14, 67108864 bytes)
[ 0.046678] Inode-cache hash table entries: 4194304 (order: 13, 33554432 bytes)
[ 0.046934] Mount-cache hash table entries: 131072 (order: 8, 1048576 bytes)
[ 0.047162] Mountpoint-cache hash table entries: 131072 (order: 8, 1048576 bytes)
[ 0.047496] CPU: Physical Processor ID: 0
[ 0.047496] CPU: Processor Core ID: 0
[ 0.047506] ENERGY_PERF_BIAS: Set to 'normal', was 'performance'
[ 0.047506] ENERGY_PERF_BIAS: View and update with x86_energy_perf_policy(8)
[ 0.047511] mce: CPU supports 9 MCE banks
[ 0.047519] CPU0: Thermal monitoring enabled (TM1)
[ 0.047532] process: using mwait in idle threads
[ 0.047535] Last level iTLB entries: 4KB 512, 2MB 7, 4MB 7
[ 0.047535] Last level dTLB entries: 4KB 512, 2MB 32, 4MB 32, 1GB 0
[ 0.047537] Spectre V2 : Mitigation: Full generic retpoline
[ 0.053359] Freeing SMP alternatives memory: 36K
[ 0.060000] smpboot: CPU0: Intel(R) Xeon(R) CPU X5675 @ 3.07GHz (family: 0x6, model: 0x2c, stepping: 0x2)
[ 0.060000] Performance Events: PEBS fmt1+, Westmere events, 16-deep LBR, Intel PMU driver.
[ 0.060000] core: CPUID marked event: 'bus cycles' unavailable
[ 0.060000] ... version: 3
[ 0.060000] ... bit width: 48
[ 0.060000] ... generic registers: 4
[ 0.060000] ... value mask: 0000ffffffffffff
[ 0.060000] ... max period: 000000007fffffff
[ 0.060000] ... fixed-purpose events: 3
[ 0.060000] ... event mask: 000000070000000f
[ 0.060000] Hierarchical SRCU implementation.
[ 0.060000] smp: Bringing up secondary CPUs ...
[ 0.060000] x86: Booting SMP configuration:
[ 0.060000] .... node #0, CPUs: #1
[ 0.060909] NMI watchdog: Enabled. Permanently consumes one hw-PMU counter.
[ 0.060936] #2 #3 #4 #5
[ 0.072182] .... node #1, CPUs: #6 #7 #8 #9 #10 #11
[ 0.170361] .... node #0, CPUs: #12 #13 #14 #15 #16 #17
[ 0.186563] .... node #1, CPUs: #18 #19 #20 #21 #22 #23
[ 0.204121] smp: Brought up 2 nodes, 24 CPUs
[ 0.204121] smpboot: Max logical packages: 2
[ 0.204121] smpboot: Total of 24 processors activated (147204.67 BogoMIPS)
[ 0.210156] devtmpfs: initialized
[ 0.210156] x86/mm: Memory block size: 128MB
[ 0.214689] evm: security.selinux
[ 0.214690] evm: security.SMACK64
[ 0.214691] evm: security.SMACK64EXEC
[ 0.214691] evm: security.SMACK64TRANSMUTE
[ 0.214691] evm: security.SMACK64MMAP
[ 0.214692] evm: security.apparmor
[ 0.214692] evm: security.ima
[ 0.214693] evm: security.capability
[ 0.214716] PM: Registering ACPI NVS region [mem 0xbf77e000-0xbf7cffff] (335872 bytes)
[ 0.214716] clocksource: jiffies: mask: 0xffffffff max_cycles: 0xffffffff, max_idle_ns: 7645041785100000 ns
[ 0.214716] futex hash table entries: 8192 (order: 7, 524288 bytes)
[ 0.214716] pinctrl core: initialized pinctrl subsystem
[ 0.214716] RTC time: 9:55:19, date: 05/24/18
[ 0.216620] NET: Registered protocol family 16
[ 0.216719] audit: initializing netlink subsys (disabled)
[ 0.216725] audit: type=2000 audit(1527155719.216:1): state=initialized audit_enabled=0 res=1
[ 0.216725] cpuidle: using governor ladder
[ 0.216725] cpuidle: using governor menu
[ 0.216725] ACPI: bus type PCI registered
[ 0.216725] acpiphp: ACPI Hot Plug PCI Controller Driver version: 0.5
[ 0.216725] PCI: MMCONFIG for domain 0000 [bus 00-ff] at [mem 0xe0000000-0xefffffff] (base 0xe0000000)
[ 0.216725] PCI: MMCONFIG at [mem 0xe0000000-0xefffffff] reserved in E820
[ 0.216725] PCI: Using configuration type 1 for base access
[ 0.218075] HugeTLB registered 1.00 GiB page size, pre-allocated 0 pages
[ 0.218075] HugeTLB registered 2.00 MiB page size, pre-allocated 0 pages
[ 0.218075] ACPI: Added _OSI(Module Device)
[ 0.218075] ACPI: Added _OSI(Processor Device)
[ 0.218075] ACPI: Added _OSI(3.0 _SCP Extensions)
[ 0.218075] ACPI: Added _OSI(Processor Aggregator Device)
[ 0.218075] ACPI: Added _OSI(Linux-Dell-Video)
[ 0.225298] ACPI: 2 ACPI AML tables successfully acquired and loaded
[ 0.228913] ACPI: Dynamic OEM Table Load:
[ 0.228913] ACPI: SSDT 0xFFFF9D6B63438000 00666C (v01 DpgPmm P001Ist 00000011 INTL 20051117)
[ 0.234561] ACPI: Dynamic OEM Table Load:
[ 0.234567] ACPI: SSDT 0xFFFF9D657BB82000 000C88 (v01 PmRef P001Cst 00003001 INTL 20051117)
[ 0.236590] ACPI: Interpreter enabled
[ 0.236608] ACPI: (supports S0 S1 S3 S4 S5)
[ 0.236609] ACPI: Using IOAPIC for interrupt routing
[ 0.236646] PCI: Using host bridge windows from ACPI; if necessary, use "pci=nocrs" and report a bug
[ 0.236938] ACPI: Enabled 13 GPEs in block 00 to 3F
[ 0.247767] ACPI: PCI Root Bridge [PCI0] (domain 0000 [bus 00-7f])
[ 0.247772] acpi PNP0A08:00: _OSC: OS supports [ExtendedConfig ASPM ClockPM Segments MSI]
[ 0.247776] acpi PNP0A08:00: _OSC failed (AE_NOT_FOUND); disabling ASPM
[ 0.248515] PCI host bridge to bus 0000:00
[ 0.248518] pci_bus 0000:00: root bus resource [io 0x0000-0x03af window]
[ 0.248519] pci_bus 0000:00: root bus resource [io 0x03e0-0x0cf7 window]
[ 0.248520] pci_bus 0000:00: root bus resource [io 0x03b0-0x03bb window]
[ 0.248521] pci_bus 0000:00: root bus resource [io 0x03c0-0x03df window]
[ 0.248523] pci_bus 0000:00: root bus resource [io 0x0d00-0xefff window]
[ 0.248524] pci_bus 0000:00: root bus resource [mem 0x000a0000-0x000bffff window]
[ 0.248525] pci_bus 0000:00: root bus resource [mem 0x000d0000-0x000dffff window]
[ 0.248526] pci_bus 0000:00: root bus resource [mem 0xf4000000-0xfbffffff window]
[ 0.248528] pci_bus 0000:00: root bus resource [mem 0xfecc000000-0xffffffffff window]
[ 0.248529] pci_bus 0000:00: root bus resource [bus 00-7f]
[ 0.248540] pci 0000:00:00.0: [8086:3406] type 00 class 0x060000
[ 0.248569] pci 0000:00:00.0: enabling Extended Tags
[ 0.248600] pci 0000:00:00.0: PME# supported from D0 D3hot D3cold
[ 0.248703] pci 0000:00:01.0: [8086:3408] type 01 class 0x060400
[ 0.248725] pci 0000:00:01.0: enabling Extended Tags
[ 0.248757] pci 0000:00:01.0: PME# supported from D0 D3hot D3cold
[ 0.248863] pci 0000:00:03.0: [8086:340a] type 01 class 0x060400
[ 0.248888] pci 0000:00:03.0: enabling Extended Tags
[ 0.248920] pci 0000:00:03.0: PME# supported from D0 D3hot D3cold
[ 0.249029] pci 0000:00:05.0: [8086:340c] type 01 class 0x060400
[ 0.249050] pci 0000:00:05.0: enabling Extended Tags
[ 0.249081] pci 0000:00:05.0: PME# supported from D0 D3hot D3cold
[ 0.249185] pci 0000:00:07.0: [8086:340e] type 01 class 0x060400
[ 0.249210] pci 0000:00:07.0: enabling Extended Tags
[ 0.249243] pci 0000:00:07.0: PME# supported from D0 D3hot D3cold
[ 0.249350] pci 0000:00:09.0: [8086:3410] type 01 class 0x060400
[ 0.249370] pci 0000:00:09.0: enabling Extended Tags
[ 0.249401] pci 0000:00:09.0: PME# supported from D0 D3hot D3cold
[ 0.249509] pci 0000:00:14.0: [8086:342e] type 00 class 0x080000
[ 0.249639] pci 0000:00:14.1: [8086:3422] type 00 class 0x080000
[ 0.249768] pci 0000:00:14.2: [8086:3423] type 00 class 0x080000
[ 0.249898] pci 0000:00:14.3: [8086:3438] type 00 class 0x080000
[ 0.250015] pci 0000:00:1a.0: [8086:3a37] type 00 class 0x0c0300
[ 0.250055] pci 0000:00:1a.0: reg 0x20: [io 0x9400-0x941f]
[ 0.250184] pci 0000:00:1a.1: [8086:3a38] type 00 class 0x0c0300
[ 0.250224] pci 0000:00:1a.1: reg 0x20: [io 0x9480-0x949f]
[ 0.250350] pci 0000:00:1a.2: [8086:3a39] type 00 class 0x0c0300
[ 0.250389] pci 0000:00:1a.2: reg 0x20: [io 0x9800-0x981f]
[ 0.250530] pci 0000:00:1a.7: [8086:3a3c] type 00 class 0x0c0320
[ 0.250550] pci 0000:00:1a.7: reg 0x10: [mem 0xf7bf8000-0xf7bf83ff]
[ 0.250626] pci 0000:00:1a.7: PME# supported from D0 D3hot D3cold
[ 0.250729] pci 0000:00:1b.0: [8086:3a3e] type 00 class 0x040300
[ 0.250747] pci 0000:00:1b.0: reg 0x10: [mem 0xf7bf4000-0xf7bf7fff 64bit]
[ 0.250812] pci 0000:00:1b.0: PME# supported from D0 D3hot D3cold
[ 0.250910] pci 0000:00:1c.0: [8086:3a40] type 01 class 0x060400
[ 0.250973] pci 0000:00:1c.0: PME# supported from D0 D3hot D3cold
[ 0.251086] pci 0000:00:1c.4: [8086:3a48] type 01 class 0x060400
[ 0.251154] pci 0000:00:1c.4: PME# supported from D0 D3hot D3cold
[ 0.251260] pci 0000:00:1c.5: [8086:3a4a] type 01 class 0x060400
[ 0.251329] pci 0000:00:1c.5: PME# supported from D0 D3hot D3cold
[ 0.251438] pci 0000:00:1d.0: [8086:3a34] type 00 class 0x0c0300
[ 0.251477] pci 0000:00:1d.0: reg 0x20: [io 0x9880-0x989f]
[ 0.251606] pci 0000:00:1d.1: [8086:3a35] type 00 class 0x0c0300
[ 0.251645] pci 0000:00:1d.1: reg 0x20: [io 0x9c00-0x9c1f]
[ 0.251774] pci 0000:00:1d.2: [8086:3a36] type 00 class 0x0c0300
[ 0.251814] pci 0000:00:1d.2: reg 0x20: [io 0xa000-0xa01f]
[ 0.251946] pci 0000:00:1d.7: [8086:3a3a] type 00 class 0x0c0320
[ 0.251966] pci 0000:00:1d.7: reg 0x10: [mem 0xf7bfa000-0xf7bfa3ff]
[ 0.252046] pci 0000:00:1d.7: PME# supported from D0 D3hot D3cold
[ 0.252145] pci 0000:00:1e.0: [8086:244e] type 01 class 0x060401
[ 0.252280] pci 0000:00:1f.0: [8086:3a16] type 00 class 0x060100
[ 0.252356] pci 0000:00:1f.0: quirk: [io 0x0800-0x087f] claimed by ICH6 ACPI/GPIO/TCO
[ 0.252359] pci 0000:00:1f.0: quirk: [io 0x0500-0x053f] claimed by ICH6 GPIO
[ 0.252362] pci 0000:00:1f.0: ICH7 LPC Generic IO decode 1 PIO at 0a00 (mask 00ff)
[ 0.252365] pci 0000:00:1f.0: ICH7 LPC Generic IO decode 2 PIO at 0ca0 (mask 000f)
[ 0.252367] pci 0000:00:1f.0: ICH7 LPC Generic IO decode 3 PIO at f700 (mask 000f)
[ 0.252489] pci 0000:00:1f.2: [8086:3a22] type 00 class 0x010601
[ 0.252505] pci 0000:00:1f.2: reg 0x10: [io 0xa080-0xa087]
[ 0.252512] pci 0000:00:1f.2: reg 0x14: [io 0xa880-0xa883]
[ 0.252518] pci 0000:00:1f.2: reg 0x18: [io 0xa800-0xa807]
[ 0.252524] pci 0000:00:1f.2: reg 0x1c: [io 0xa480-0xa483]
[ 0.252531] pci 0000:00:1f.2: reg 0x20: [io 0xa400-0xa41f]
[ 0.252537] pci 0000:00:1f.2: reg 0x24: [mem 0xf7bfc000-0xf7bfc7ff]
[ 0.252574] pci 0000:00:1f.2: PME# supported from D3hot
[ 0.252678] pci 0000:00:1f.3: [8086:3a30] type 00 class 0x0c0500
[ 0.252694] pci 0000:00:1f.3: reg 0x10: [mem 0xf7bfe000-0xf7bfe0ff 64bit]
[ 0.252712] pci 0000:00:1f.3: reg 0x20: [io 0x0400-0x041f]
[ 0.252841] pci 0000:00:01.0: PCI bridge to [bus 09]
[ 0.252884] pci 0000:08:00.0: [10de:1c82] type 00 class 0x030000
[ 0.252903] pci 0000:08:00.0: reg 0x10: [mem 0xf8000000-0xf8ffffff]
[ 0.252913] pci 0000:08:00.0: reg 0x14: [mem 0xfef0000000-0xfeffffffff 64bit pref]
[ 0.252923] pci 0000:08:00.0: reg 0x1c: [mem 0xfeee000000-0xfeefffffff 64bit pref]
[ 0.252930] pci 0000:08:00.0: reg 0x24: [io 0xec00-0xec7f]
[ 0.252937] pci 0000:08:00.0: reg 0x30: [mem 0xf7f80000-0xf7ffffff pref]
[ 0.253052] pci 0000:08:00.1: [10de:0fb9] type 00 class 0x040300
[ 0.253067] pci 0000:08:00.1: reg 0x10: [mem 0xfbefc000-0xfbefffff]
[ 0.253194] pci 0000:00:03.0: PCI bridge to [bus 08]
[ 0.253196] pci 0000:00:03.0: bridge window [io 0xe000-0xefff]
[ 0.253199] pci 0000:00:03.0: bridge window [mem 0xf7f00000-0xfbefffff]
[ 0.253202] pci 0000:00:03.0: bridge window [mem 0xfeee000000-0xfeffffffff 64bit pref]
[ 0.253238] pci 0000:00:05.0: PCI bridge to [bus 07]
[ 0.253284] pci 0000:06:00.0: [1002:67ff] type 00 class 0x030000
[ 0.253316] pci 0000:06:00.0: reg 0x10: [mem 0xfed0000000-0xfedfffffff 64bit pref]
[ 0.253327] pci 0000:06:00.0: reg 0x18: [mem 0xfecfe00000-0xfecfffffff 64bit pref]
[ 0.253334] pci 0000:06:00.0: reg 0x20: [io 0xd000-0xd0ff]
[ 0.253341] pci 0000:06:00.0: reg 0x24: [mem 0xf7e80000-0xf7ebffff]
[ 0.253348] pci 0000:06:00.0: reg 0x30: [mem 0xf7e60000-0xf7e7ffff pref]
[ 0.253355] pci 0000:06:00.0: enabling Extended Tags
[ 0.253432] pci 0000:06:00.0: supports D1 D2
[ 0.253433] pci 0000:06:00.0: PME# supported from D1 D2 D3hot D3cold
[ 0.253542] pci 0000:06:00.1: [1002:aae0] type 00 class 0x040300
[ 0.253570] pci 0000:06:00.1: reg 0x10: [mem 0xf7efc000-0xf7efffff 64bit]
[ 0.253615] pci 0000:06:00.1: enabling Extended Tags
[ 0.253673] pci 0000:06:00.1: supports D1 D2
[ 0.253753] pci 0000:00:07.0: PCI bridge to [bus 06]
[ 0.253755] pci 0000:00:07.0: bridge window [io 0xd000-0xdfff]
[ 0.253758] pci 0000:00:07.0: bridge window [mem 0xf7e00000-0xf7efffff]
[ 0.253761] pci 0000:00:07.0: bridge window [mem 0xfecfe00000-0xfedfffffff 64bit pref]
[ 0.253794] pci 0000:00:09.0: PCI bridge to [bus 05]
[ 0.253846] pci 0000:00:1c.0: PCI bridge to [bus 04]
[ 0.253917] pci 0000:03:00.0: [8086:10d3] type 00 class 0x020000
[ 0.253955] pci 0000:03:00.0: reg 0x10: [mem 0xf7de0000-0xf7dfffff]
[ 0.253985] pci 0000:03:00.0: reg 0x18: [io 0xcc00-0xcc1f]
[ 0.254001] pci 0000:03:00.0: reg 0x1c: [mem 0xf7ddc000-0xf7ddffff]
[ 0.254140] pci 0000:03:00.0: PME# supported from D0 D3hot D3cold
[ 0.254244] pci 0000:00:1c.4: ASPM: current common clock configuration is broken, reconfiguring
[ 0.264025] pci 0000:00:1c.4: PCI bridge to [bus 03]
[ 0.264030] pci 0000:00:1c.4: bridge window [io 0xc000-0xcfff]
[ 0.264034] pci 0000:00:1c.4: bridge window [mem 0xf7d00000-0xf7dfffff]
[ 0.264121] pci 0000:02:00.0: [8086:10d3] type 00 class 0x020000
[ 0.264159] pci 0000:02:00.0: reg 0x10: [mem 0xf7ce0000-0xf7cfffff]
[ 0.264189] pci 0000:02:00.0: reg 0x18: [io 0xbc00-0xbc1f]
[ 0.264205] pci 0000:02:00.0: reg 0x1c: [mem 0xf7cdc000-0xf7cdffff]
[ 0.264345] pci 0000:02:00.0: PME# supported from D0 D3hot D3cold
[ 0.264447] pci 0000:00:1c.5: ASPM: current common clock configuration is broken, reconfiguring
[ 0.276024] pci 0000:00:1c.5: PCI bridge to [bus 02]
[ 0.276029] pci 0000:00:1c.5: bridge window [io 0xb000-0xbfff]
[ 0.276033] pci 0000:00:1c.5: bridge window [mem 0xf7c00000-0xf7cfffff]
[ 0.276112] pci 0000:00:1e.0: PCI bridge to [bus 01] (subtractive decode)
[ 0.276119] pci 0000:00:1e.0: bridge window [io 0x0000-0x03af window] (subtractive decode)
[ 0.276121] pci 0000:00:1e.0: bridge window [io 0x03e0-0x0cf7 window] (subtractive decode)
[ 0.276122] pci 0000:00:1e.0: bridge window [io 0x03b0-0x03bb window] (subtractive decode)
[ 0.276123] pci 0000:00:1e.0: bridge window [io 0x03c0-0x03df window] (subtractive decode)
[ 0.276124] pci 0000:00:1e.0: bridge window [io 0x0d00-0xefff window] (subtractive decode)
[ 0.276126] pci 0000:00:1e.0: bridge window [mem 0x000a0000-0x000bffff window] (subtractive decode)
[ 0.276127] pci 0000:00:1e.0: bridge window [mem 0x000d0000-0x000dffff window] (subtractive decode)
[ 0.276128] pci 0000:00:1e.0: bridge window [mem 0xf4000000-0xfbffffff window] (subtractive decode)
[ 0.276129] pci 0000:00:1e.0: bridge window [mem 0xfecc000000-0xffffffffff window] (subtractive decode)
[ 0.277224] ACPI: PCI Root Bridge [BR50] (domain 0000 [bus 80-fb])
[ 0.277229] acpi PNP0A08:01: _OSC: OS supports [ExtendedConfig ASPM ClockPM Segments MSI]
[ 0.277233] acpi PNP0A08:01: _OSC failed (AE_NOT_FOUND); disabling ASPM
[ 0.277698] acpi PNP0A08:01: host bridge window [io 0x0000 window] (ignored, not CPU addressable)
[ 0.277834] PCI host bridge to bus 0000:80
[ 0.277836] pci_bus 0000:80: root bus resource [mem 0xf0000000-0xf3ffffff window]
[ 0.277837] pci_bus 0000:80: root bus resource [mem 0xfec8000000-0xfecbffffff window]
[ 0.277839] pci_bus 0000:80: root bus resource [bus 80-fb]
[ 0.277850] pci 0000:80:00.0: [8086:3420] type 01 class 0x060400
[ 0.277876] pci 0000:80:00.0: enabling Extended Tags
[ 0.277914] pci 0000:80:00.0: PME# supported from D0 D3hot D3cold
[ 0.277992] pci 0000:80:01.0: [8086:3408] type 01 class 0x060400
[ 0.278019] pci 0000:80:01.0: enabling Extended Tags
[ 0.278060] pci 0000:80:01.0: PME# supported from D0 D3hot D3cold
[ 0.278140] pci 0000:80:03.0: [8086:340a] type 01 class 0x060400
[ 0.278167] pci 0000:80:03.0: enabling Extended Tags
[ 0.278207] pci 0000:80:03.0: PME# supported from D0 D3hot D3cold
[ 0.278290] pci 0000:80:07.0: [8086:340e] type 01 class 0x060400
[ 0.278321] pci 0000:80:07.0: enabling Extended Tags
[ 0.278362] pci 0000:80:07.0: PME# supported from D0 D3hot D3cold
[ 0.278444] pci 0000:80:10.0: [8086:3425] type 00 class 0x080000
[ 0.278542] pci 0000:80:10.1: [8086:3426] type 00 class 0x080000
[ 0.278632] pci 0000:80:11.0: [8086:3427] type 00 class 0x080000
[ 0.278728] pci 0000:80:11.1: [8086:3428] type 00 class 0x080000
[ 0.278826] pci 0000:80:14.0: [8086:342e] type 00 class 0x080000
[ 0.278936] pci 0000:80:14.1: [8086:3422] type 00 class 0x080000
[ 0.279044] pci 0000:80:14.2: [8086:3423] type 00 class 0x080000
[ 0.279150] pci 0000:80:14.3: [8086:3438] type 00 class 0x080000
[ 0.279263] pci 0000:80:00.0: PCI bridge to [bus 84]
[ 0.279304] pci 0000:80:01.0: PCI bridge to [bus 83]
[ 0.279343] pci 0000:80:03.0: PCI bridge to [bus 82]
[ 0.279389] pci 0000:81:00.0: [144d:a804] type 00 class 0x010802
[ 0.279411] pci 0000:81:00.0: reg 0x10: [mem 0xf3ffc000-0xf3ffffff 64bit]
[ 0.288035] pci 0000:80:07.0: PCI bridge to [bus 81]
[ 0.288042] pci 0000:80:07.0: bridge window [mem 0xf3f00000-0xf3ffffff]
[ 0.288197] ACPI: PCI Interrupt Link [LNKA] (IRQs 3 4 6 7 *10 11 12 14 15)
[ 0.288266] ACPI: PCI Interrupt Link [LNKB] (IRQs *5)
[ 0.288333] ACPI: PCI Interrupt Link [LNKC] (IRQs 3 4 6 7 10 11 12 14 *15)
[ 0.288401] ACPI: PCI Interrupt Link [LNKD] (IRQs 3 4 6 7 10 *11 12 14 15)
[ 0.288468] ACPI: PCI Interrupt Link [LNKE] (IRQs 3 4 6 7 10 11 12 14 15) *0, disabled.
[ 0.288537] ACPI: PCI Interrupt Link [LNKF] (IRQs 3 4 *6 7 10 11 12 14 15)
[ 0.288605] ACPI: PCI Interrupt Link [LNKG] (IRQs 3 4 6 *7 10 11 12 14 15)
[ 0.288673] ACPI: PCI Interrupt Link [LNKH] (IRQs 3 4 6 7 10 11 12 *14 15)
[ 0.288815] pci 0000:08:00.0: vgaarb: setting as boot VGA device
[ 0.288815] pci 0000:08:00.0: vgaarb: VGA device added: decodes=io+mem,owns=io+mem,locks=none
[ 0.288815] pci 0000:06:00.0: vgaarb: VGA device added: decodes=io+mem,owns=none,locks=none
[ 0.288815] pci 0000:06:00.0: vgaarb: bridge control possible
[ 0.288815] pci 0000:08:00.0: vgaarb: bridge control possible
[ 0.288815] vgaarb: loaded
[ 0.288815] SCSI subsystem initialized
[ 0.288815] libata version 3.00 loaded.
[ 0.288815] ACPI: bus type USB registered
[ 0.288815] usbcore: registered new interface driver usbfs
[ 0.288815] usbcore: registered new interface driver hub
[ 0.288815] usbcore: registered new device driver usb
[ 0.288815] pps_core: LinuxPPS API ver. 1 registered
[ 0.288815] pps_core: Software ver. 5.3.6 - Copyright 2005-2007 Rodolfo Giometti <giometti@linux.it>
[ 0.288815] PTP clock support registered
[ 0.288815] EDAC MC: Ver: 3.0.0
[ 0.288815] PCI: Using ACPI for IRQ routing
[ 0.292304] PCI: Discovered peer bus fe
[ 0.292309] PCI: root bus fe: using default resources
[ 0.292310] PCI: Probing PCI hardware (bus fe)
[ 0.292348] PCI host bridge to bus 0000:fe
[ 0.292350] pci_bus 0000:fe: root bus resource [io 0x0000-0xffff]
[ 0.292352] pci_bus 0000:fe: root bus resource [mem 0x00000000-0xffffffffff]
[ 0.292353] pci_bus 0000:fe: No busn resource found for root bus, will use [bus fe-ff]
[ 0.292358] pci 0000:fe:00.0: [8086:2c70] type 00 class 0x060000
[ 0.292402] pci 0000:fe:00.1: [8086:2d81] type 00 class 0x060000
[ 0.292442] pci 0000:fe:02.0: [8086:2d90] type 00 class 0x060000
[ 0.292484] pci 0000:fe:02.1: [8086:2d91] type 00 class 0x060000
[ 0.292522] pci 0000:fe:02.2: [8086:2d92] type 00 class 0x060000
[ 0.292562] pci 0000:fe:02.3: [8086:2d93] type 00 class 0x060000
[ 0.292600] pci 0000:fe:02.4: [8086:2d94] type 00 class 0x060000
[ 0.292638] pci 0000:fe:02.5: [8086:2d95] type 00 class 0x060000
[ 0.292682] pci 0000:fe:03.0: [8086:2d98] type 00 class 0x060000
[ 0.292721] pci 0000:fe:03.1: [8086:2d99] type 00 class 0x060000
[ 0.292759] pci 0000:fe:03.2: [8086:2d9a] type 00 class 0x060000
[ 0.292797] pci 0000:fe:03.4: [8086:2d9c] type 00 class 0x060000
[ 0.292836] pci 0000:fe:04.0: [8086:2da0] type 00 class 0x060000
[ 0.292879] pci 0000:fe:04.1: [8086:2da1] type 00 class 0x060000
[ 0.292916] pci 0000:fe:04.2: [8086:2da2] type 00 class 0x060000
[ 0.292953] pci 0000:fe:04.3: [8086:2da3] type 00 class 0x060000
[ 0.292992] pci 0000:fe:05.0: [8086:2da8] type 00 class 0x060000
[ 0.293029] pci 0000:fe:05.1: [8086:2da9] type 00 class 0x060000
[ 0.293067] pci 0000:fe:05.2: [8086:2daa] type 00 class 0x060000
[ 0.293103] pci 0000:fe:05.3: [8086:2dab] type 00 class 0x060000
[ 0.293142] pci 0000:fe:06.0: [8086:2db0] type 00 class 0x060000
[ 0.293178] pci 0000:fe:06.1: [8086:2db1] type 00 class 0x060000
[ 0.293214] pci 0000:fe:06.2: [8086:2db2] type 00 class 0x060000
[ 0.293253] pci 0000:fe:06.3: [8086:2db3] type 00 class 0x060000
[ 0.293301] pci_bus 0000:fe: busn_res: [bus fe-ff] end is updated to fe
[ 0.293308] PCI: Discovered peer bus ff
[ 0.293308] PCI: root bus ff: using default resources
[ 0.293309] PCI: Probing PCI hardware (bus ff)
[ 0.293328] PCI host bridge to bus 0000:ff
[ 0.293329] pci_bus 0000:ff: root bus resource [io 0x0000-0xffff]
[ 0.293331] pci_bus 0000:ff: root bus resource [mem 0x00000000-0xffffffffff]
[ 0.293332] pci_bus 0000:ff: No busn resource found for root bus, will use [bus ff-ff]
[ 0.293336] pci 0000:ff:00.0: [8086:2c70] type 00 class 0x060000
[ 0.293371] pci 0000:ff:00.1: [8086:2d81] type 00 class 0x060000
[ 0.293407] pci 0000:ff:02.0: [8086:2d90] type 00 class 0x060000
[ 0.293446] pci 0000:ff:02.1: [8086:2d91] type 00 class 0x060000
[ 0.293482] pci 0000:ff:02.2: [8086:2d92] type 00 class 0x060000
[ 0.293516] pci 0000:ff:02.3: [8086:2d93] type 00 class 0x060000
[ 0.293550] pci 0000:ff:02.4: [8086:2d94] type 00 class 0x060000
[ 0.293584] pci 0000:ff:02.5: [8086:2d95] type 00 class 0x060000
[ 0.293620] pci 0000:ff:03.0: [8086:2d98] type 00 class 0x060000
[ 0.293655] pci 0000:ff:03.1: [8086:2d99] type 00 class 0x060000
[ 0.293689] pci 0000:ff:03.2: [8086:2d9a] type 00 class 0x060000
[ 0.293724] pci 0000:ff:03.4: [8086:2d9c] type 00 class 0x060000
[ 0.293759] pci 0000:ff:04.0: [8086:2da0] type 00 class 0x060000
[ 0.293793] pci 0000:ff:04.1: [8086:2da1] type 00 class 0x060000
[ 0.293830] pci 0000:ff:04.2: [8086:2da2] type 00 class 0x060000
[ 0.293864] pci 0000:ff:04.3: [8086:2da3] type 00 class 0x060000
[ 0.293904] pci 0000:ff:05.0: [8086:2da8] type 00 class 0x060000
[ 0.293938] pci 0000:ff:05.1: [8086:2da9] type 00 class 0x060000
[ 0.293972] pci 0000:ff:05.2: [8086:2daa] type 00 class 0x060000
[ 0.294008] pci 0000:ff:05.3: [8086:2dab] type 00 class 0x060000
[ 0.294046] pci 0000:ff:06.0: [8086:2db0] type 00 class 0x060000
[ 0.294081] pci 0000:ff:06.1: [8086:2db1] type 00 class 0x060000
[ 0.294115] pci 0000:ff:06.2: [8086:2db2] type 00 class 0x060000
[ 0.294149] pci 0000:ff:06.3: [8086:2db3] type 00 class 0x060000
[ 0.294195] pci_bus 0000:ff: busn_res: [bus ff] end is updated to ff
[ 0.294201] PCI: pci_cache_line_size set to 64 bytes
[ 0.294326] e820: reserve RAM buffer [mem 0x0009d400-0x0009ffff]
[ 0.294327] e820: reserve RAM buffer [mem 0xbf770000-0xbfffffff]
[ 0.294433] NetLabel: Initializing
[ 0.294434] NetLabel: domain hash size = 128
[ 0.294434] NetLabel: protocols = UNLABELED CIPSOv4 CALIPSO
[ 0.294448] NetLabel: unlabeled traffic allowed by default
[ 0.296067] hpet0: at MMIO 0xfed00000, IRQs 2, 8, 0, 0
[ 0.296071] hpet0: 4 comparators, 64-bit 14.318180 MHz counter
[ 0.297047] clocksource: Switched to clocksource tsc-early
[ 0.310095] VFS: Disk quotas dquot_6.6.0
[ 0.310123] VFS: Dquot-cache hash table entries: 512 (order 0, 4096 bytes)
[ 0.310273] AppArmor: AppArmor Filesystem Enabled
[ 0.310299] pnp: PnP ACPI init
[ 0.310408] system 00:00: [mem 0xfbf00000-0xfbffffff] has been reserved
[ 0.310410] system 00:00: [mem 0xfc000000-0xfcffffff] has been reserved
[ 0.310412] system 00:00: [mem 0xfd000000-0xfdffffff] has been reserved
[ 0.310418] system 00:00: [mem 0xfe000000-0xfebfffff] has been reserved
[ 0.310419] system 00:00: [mem 0xfed10000-0xfed10fff] has been reserved
[ 0.310424] system 00:00: Plug and Play ACPI device, IDs PNP0c01 (active)
[ 0.310505] pnp 00:01: Plug and Play ACPI device, IDs PNP0b00 (active)
[ 0.310801] pnp 00:02: [dma 0 disabled]
[ 0.310860] pnp 00:02: Plug and Play ACPI device, IDs PNP0501 (active)
[ 0.311099] pnp 00:03: [dma 0 disabled]
[ 0.311177] pnp 00:03: Plug and Play ACPI device, IDs PNP0501 (active)
[ 0.311346] system 00:04: [io 0x0a00-0x0a0f] has been reserved
[ 0.311348] system 00:04: [io 0x0a10-0x0a1f] has been reserved
[ 0.311352] system 00:04: Plug and Play ACPI device, IDs PNP0c02 (active)
[ 0.311561] system 00:05: [io 0x04d0-0x04d1] has been reserved
[ 0.311563] system 00:05: [io 0x0800-0x087f] has been reserved
[ 0.311564] system 00:05: [io 0x0500-0x057f] could not be reserved
[ 0.311566] system 00:05: [mem 0xfed1c000-0xfed1ffff] has been reserved
[ 0.311568] system 00:05: [mem 0xfed20000-0xfed3ffff] has been reserved
[ 0.311570] system 00:05: [mem 0xfed40000-0xfed8ffff] has been reserved
[ 0.311574] system 00:05: Plug and Play ACPI device, IDs PNP0c02 (active)
[ 0.311764] system 00:06: [mem 0xfec00000-0xfec00fff] could not be reserved
[ 0.311766] system 00:06: [mem 0xfee00000-0xfee00fff] has been reserved
[ 0.311770] system 00:06: Plug and Play ACPI device, IDs PNP0c02 (active)
[ 0.311876] system 00:07: [mem 0xe0000000-0xefffffff] has been reserved
[ 0.311880] system 00:07: Plug and Play ACPI device, IDs PNP0c02 (active)
[ 0.312127] system 00:08: [mem 0x00000000-0x0009ffff] could not be reserved
[ 0.312129] system 00:08: [mem 0x000c0000-0x000cffff] could not be reserved
[ 0.312130] system 00:08: [mem 0x000e0000-0x000fffff] could not be reserved
[ 0.312132] system 00:08: [mem 0x00100000-0xbfffffff] could not be reserved
[ 0.312134] system 00:08: [mem 0xfed90000-0xffffffff] could not be reserved
[ 0.312138] system 00:08: Plug and Play ACPI device, IDs PNP0c01 (active)
[ 0.312228] system 00:09: Plug and Play ACPI device, IDs PNP0c01 (active)
[ 0.312398] pnp: PnP ACPI: found 10 devices
[ 0.318274] clocksource: acpi_pm: mask: 0xffffff max_cycles: 0xffffff, max_idle_ns: 2085701024 ns
[ 0.318313] pci 0000:00:1c.0: bridge window [io 0x1000-0x0fff] to [bus 04] add_size 1000
[ 0.318315] pci 0000:00:1c.0: bridge window [mem 0x00100000-0x000fffff 64bit pref] to [bus 04] add_size 200000 add_align 100000
[ 0.318317] pci 0000:00:1c.0: bridge window [mem 0x00100000-0x000fffff] to [bus 04] add_size 200000 add_align 100000
[ 0.318323] pci 0000:00:1c.4: bridge window [mem 0x00100000-0x000fffff 64bit pref] to [bus 03] add_size 200000 add_align 100000
[ 0.318333] pci 0000:00:1c.5: bridge window [mem 0x00100000-0x000fffff 64bit pref] to [bus 02] add_size 200000 add_align 100000
[ 0.318348] pci 0000:00:1c.0: BAR 14: assigned [mem 0xf4000000-0xf41fffff]
[ 0.318351] pci 0000:00:1c.0: BAR 15: assigned [mem 0xfecc000000-0xfecc1fffff 64bit pref]
[ 0.318354] pci 0000:00:1c.4: BAR 15: assigned [mem 0xfecc200000-0xfecc3fffff 64bit pref]
[ 0.318357] pci 0000:00:1c.5: BAR 15: assigned [mem 0xfecc400000-0xfecc5fffff 64bit pref]
[ 0.318359] pci 0000:00:1c.0: BAR 13: assigned [io 0x1000-0x1fff]
[ 0.318362] pci 0000:00:01.0: PCI bridge to [bus 09]
[ 0.318369] pci 0000:00:03.0: PCI bridge to [bus 08]
[ 0.318371] pci 0000:00:03.0: bridge window [io 0xe000-0xefff]
[ 0.318374] pci 0000:00:03.0: bridge window [mem 0xf7f00000-0xfbefffff]
[ 0.318377] pci 0000:00:03.0: bridge window [mem 0xfeee000000-0xfeffffffff 64bit pref]
[ 0.318380] pci 0000:00:05.0: PCI bridge to [bus 07]
[ 0.318387] pci 0000:00:07.0: PCI bridge to [bus 06]
[ 0.318389] pci 0000:00:07.0: bridge window [io 0xd000-0xdfff]
[ 0.318392] pci 0000:00:07.0: bridge window [mem 0xf7e00000-0xf7efffff]
[ 0.318394] pci 0000:00:07.0: bridge window [mem 0xfecfe00000-0xfedfffffff 64bit pref]
[ 0.318398] pci 0000:00:09.0: PCI bridge to [bus 05]
[ 0.318405] pci 0000:00:1c.0: PCI bridge to [bus 04]
[ 0.318407] pci 0000:00:1c.0: bridge window [io 0x1000-0x1fff]
[ 0.318410] pci 0000:00:1c.0: bridge window [mem 0xf4000000-0xf41fffff]
[ 0.318413] pci 0000:00:1c.0: bridge window [mem 0xfecc000000-0xfecc1fffff 64bit pref]
[ 0.318417] pci 0000:00:1c.4: PCI bridge to [bus 03]
[ 0.318419] pci 0000:00:1c.4: bridge window [io 0xc000-0xcfff]
[ 0.318422] pci 0000:00:1c.4: bridge window [mem 0xf7d00000-0xf7dfffff]
[ 0.318425] pci 0000:00:1c.4: bridge window [mem 0xfecc200000-0xfecc3fffff 64bit pref]
[ 0.318429] pci 0000:00:1c.5: PCI bridge to [bus 02]
[ 0.318431] pci 0000:00:1c.5: bridge window [io 0xb000-0xbfff]
[ 0.318434] pci 0000:00:1c.5: bridge window [mem 0xf7c00000-0xf7cfffff]
[ 0.318437] pci 0000:00:1c.5: bridge window [mem 0xfecc400000-0xfecc5fffff 64bit pref]
[ 0.318441] pci 0000:00:1e.0: PCI bridge to [bus 01]
[ 0.318450] pci_bus 0000:00: resource 4 [io 0x0000-0x03af window]
[ 0.318451] pci_bus 0000:00: resource 5 [io 0x03e0-0x0cf7 window]
[ 0.318452] pci_bus 0000:00: resource 6 [io 0x03b0-0x03bb window]
[ 0.318454] pci_bus 0000:00: resource 7 [io 0x03c0-0x03df window]
[ 0.318455] pci_bus 0000:00: resource 8 [io 0x0d00-0xefff window]
[ 0.318456] pci_bus 0000:00: resource 9 [mem 0x000a0000-0x000bffff window]
[ 0.318457] pci_bus 0000:00: resource 10 [mem 0x000d0000-0x000dffff window]
[ 0.318458] pci_bus 0000:00: resource 11 [mem 0xf4000000-0xfbffffff window]
[ 0.318460] pci_bus 0000:00: resource 12 [mem 0xfecc000000-0xffffffffff window]
[ 0.318461] pci_bus 0000:08: resource 0 [io 0xe000-0xefff]
[ 0.318462] pci_bus 0000:08: resource 1 [mem 0xf7f00000-0xfbefffff]
[ 0.318463] pci_bus 0000:08: resource 2 [mem 0xfeee000000-0xfeffffffff 64bit pref]
[ 0.318465] pci_bus 0000:06: resource 0 [io 0xd000-0xdfff]
[ 0.318466] pci_bus 0000:06: resource 1 [mem 0xf7e00000-0xf7efffff]
[ 0.318467] pci_bus 0000:06: resource 2 [mem 0xfecfe00000-0xfedfffffff 64bit pref]
[ 0.318469] pci_bus 0000:04: resource 0 [io 0x1000-0x1fff]
[ 0.318470] pci_bus 0000:04: resource 1 [mem 0xf4000000-0xf41fffff]
[ 0.318471] pci_bus 0000:04: resource 2 [mem 0xfecc000000-0xfecc1fffff 64bit pref]
[ 0.318472] pci_bus 0000:03: resource 0 [io 0xc000-0xcfff]
[ 0.318473] pci_bus 0000:03: resource 1 [mem 0xf7d00000-0xf7dfffff]
[ 0.318475] pci_bus 0000:03: resource 2 [mem 0xfecc200000-0xfecc3fffff 64bit pref]
[ 0.318476] pci_bus 0000:02: resource 0 [io 0xb000-0xbfff]
[ 0.318477] pci_bus 0000:02: resource 1 [mem 0xf7c00000-0xf7cfffff]
[ 0.318478] pci_bus 0000:02: resource 2 [mem 0xfecc400000-0xfecc5fffff 64bit pref]
[ 0.318480] pci_bus 0000:01: resource 4 [io 0x0000-0x03af window]
[ 0.318481] pci_bus 0000:01: resource 5 [io 0x03e0-0x0cf7 window]
[ 0.318482] pci_bus 0000:01: resource 6 [io 0x03b0-0x03bb window]
[ 0.318483] pci_bus 0000:01: resource 7 [io 0x03c0-0x03df window]
[ 0.318484] pci_bus 0000:01: resource 8 [io 0x0d00-0xefff window]
[ 0.318486] pci_bus 0000:01: resource 9 [mem 0x000a0000-0x000bffff window]
[ 0.318487] pci_bus 0000:01: resource 10 [mem 0x000d0000-0x000dffff window]
[ 0.318488] pci_bus 0000:01: resource 11 [mem 0xf4000000-0xfbffffff window]
[ 0.318489] pci_bus 0000:01: resource 12 [mem 0xfecc000000-0xffffffffff window]
[ 0.318567] pci 0000:80:00.0: PCI bridge to [bus 84]
[ 0.318575] pci 0000:80:01.0: PCI bridge to [bus 83]
[ 0.318582] pci 0000:80:03.0: PCI bridge to [bus 82]
[ 0.318590] pci 0000:80:07.0: PCI bridge to [bus 81]
[ 0.318593] pci 0000:80:07.0: bridge window [mem 0xf3f00000-0xf3ffffff]
[ 0.318599] pci_bus 0000:80: resource 4 [mem 0xf0000000-0xf3ffffff window]
[ 0.318601] pci_bus 0000:80: resource 5 [mem 0xfec8000000-0xfecbffffff window]
[ 0.318602] pci_bus 0000:81: resource 1 [mem 0xf3f00000-0xf3ffffff]
[ 0.318614] pci_bus 0000:fe: resource 4 [io 0x0000-0xffff]
[ 0.318616] pci_bus 0000:fe: resource 5 [mem 0x00000000-0xffffffffff]
[ 0.318619] pci_bus 0000:ff: resource 4 [io 0x0000-0xffff]
[ 0.318620] pci_bus 0000:ff: resource 5 [mem 0x00000000-0xffffffffff]
[ 0.318667] NET: Registered protocol family 2
[ 0.318921] tcp_listen_portaddr_hash hash table entries: 32768 (order: 7, 524288 bytes)
[ 0.319128] TCP established hash table entries: 524288 (order: 10, 4194304 bytes)
[ 0.319908] TCP bind hash table entries: 65536 (order: 8, 1048576 bytes)
[ 0.320066] TCP: Hash tables configured (established 524288 bind 65536)
[ 0.320157] UDP hash table entries: 32768 (order: 8, 1048576 bytes)
[ 0.320355] UDP-Lite hash table entries: 32768 (order: 8, 1048576 bytes)
[ 0.320659] NET: Registered protocol family 1
[ 0.322498] pci 0000:08:00.0: Video device with shadowed ROM at [mem 0x000c0000-0x000dffff]
[ 0.322504] pci 0000:08:00.1: Linked as a consumer to 0000:08:00.0
[ 0.322548] pci 0000:06:00.1: Linked as a consumer to 0000:06:00.0
[ 0.322637] PCI: CLS 256 bytes, default 64
[ 0.322677] Unpacking initramfs...
[ 1.008662] Freeing initrd memory: 50016K
[ 1.008712] PCI-DMA: Using software bounce buffering for IO (SWIOTLB)
[ 1.008715] software IO TLB [mem 0xbb770000-0xbf770000] (64MB) mapped at [ (ptrval)- (ptrval)]
[ 1.009315] Scanning for low memory corruption every 60 seconds
[ 1.010180] Initialise system trusted keyrings
[ 1.010190] Key type blacklist registered
[ 1.010237] workingset: timestamp_bits=36 max_order=24 bucket_order=0
[ 1.011516] zbud: loaded
[ 1.012089] squashfs: version 4.0 (2009/01/31) Phillip Lougher
[ 1.012285] fuse init (API version 7.26)
[ 1.012349] pstore: using deflate compression
[ 1.013310] Key type asymmetric registered
[ 1.013311] Asymmetric key parser 'x509' registered
[ 1.013341] Block layer SCSI generic (bsg) driver version 0.4 loaded (major 244)
[ 1.013387] io scheduler noop registered
[ 1.013388] io scheduler deadline registered
[ 1.013435] io scheduler cfq registered (default)
[ 1.013905] pcieport 0000:00:1c.0: enabling device (0104 -> 0107)
[ 1.014653] vesafb: mode is 1280x1024x32, linelength=5120, pages=0
[ 1.014654] vesafb: scrolling: redraw
[ 1.014655] vesafb: Truecolor: size=8:8:8:8, shift=24:16:8:0
[ 1.014666] vesafb: framebuffer at 0xef000000, mapped to 0x (ptrval), using 5120k, total 5120k
[ 1.339937] Console: switching to colour frame buffer device 160x64
[ 1.665037] fb0: VESA VGA frame buffer device
[ 1.665061] intel_idle: MWAIT substates: 0x1120
[ 1.665062] intel_idle: v0.4.1 model 0x2C
[ 1.665909] intel_idle: lapic_timer_reliable_states 0xffffffff
[ 1.665997] input: Power Button as /devices/LNXSYSTM:00/LNXSYBUS:00/PNP0C0C:00/input/input0
[ 1.666017] ACPI: Power Button [PWRB]
[ 1.666050] input: Power Button as /devices/LNXSYSTM:00/LNXPWRBN:00/input/input1
[ 1.666057] ACPI: Power Button [PWRF]
[ 1.667019] Serial: 8250/16550 driver, 32 ports, IRQ sharing enabled
[ 1.687443] 00:02: ttyS0 at I/O 0x3f8 (irq = 4, base_baud = 115200) is a 16550A
[ 1.707958] 00:03: ttyS1 at I/O 0x2f8 (irq = 3, base_baud = 115200) is a 16550A
[ 1.710343] Linux agpgart interface v0.103
[ 1.718200] loop: module loaded
[ 1.718688] nvme nvme0: pci function 0000:81:00.0
[ 1.718790] libphy: Fixed MDIO Bus: probed
[ 1.718791] tun: Universal TUN/TAP device driver, 1.6
[ 1.718858] PPP generic driver version 2.4.2
[ 1.718929] ehci_hcd: USB 2.0 'Enhanced' Host Controller (EHCI) Driver
[ 1.718932] ehci-pci: EHCI PCI platform driver
[ 1.719089] ehci-pci 0000:00:1a.7: EHCI Host Controller
[ 1.719098] ehci-pci 0000:00:1a.7: new USB bus registered, assigned bus number 1
[ 1.719109] ehci-pci 0000:00:1a.7: debug port 1
[ 1.723005] ehci-pci 0000:00:1a.7: cache line size of 256 is not supported
[ 1.723017] ehci-pci 0000:00:1a.7: irq 18, io mem 0xf7bf8000
[ 1.736085] ehci-pci 0000:00:1a.7: USB 2.0 started, EHCI 1.00
[ 1.736159] usb usb1: New USB device found, idVendor=1d6b, idProduct=0002, bcdDevice= 4.17
[ 1.736162] usb usb1: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.736165] usb usb1: Product: EHCI Host Controller
[ 1.736167] usb usb1: Manufacturer: Linux 4.17.0-rc6 ehci_hcd
[ 1.736169] usb usb1: SerialNumber: 0000:00:1a.7
[ 1.736430] hub 1-0:1.0: USB hub found
[ 1.736442] hub 1-0:1.0: 6 ports detected
[ 1.736719] ehci-pci 0000:00:1d.7: EHCI Host Controller
[ 1.736723] ehci-pci 0000:00:1d.7: new USB bus registered, assigned bus number 2
[ 1.736735] ehci-pci 0000:00:1d.7: debug port 1
[ 1.740643] ehci-pci 0000:00:1d.7: cache line size of 256 is not supported
[ 1.740652] ehci-pci 0000:00:1d.7: irq 23, io mem 0xf7bfa000
[ 1.756102] ehci-pci 0000:00:1d.7: USB 2.0 started, EHCI 1.00
[ 1.756158] usb usb2: New USB device found, idVendor=1d6b, idProduct=0002, bcdDevice= 4.17
[ 1.756161] usb usb2: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.756163] usb usb2: Product: EHCI Host Controller
[ 1.756166] usb usb2: Manufacturer: Linux 4.17.0-rc6 ehci_hcd
[ 1.756168] usb usb2: SerialNumber: 0000:00:1d.7
[ 1.756408] hub 2-0:1.0: USB hub found
[ 1.756419] hub 2-0:1.0: 6 ports detected
[ 1.756564] ehci-platform: EHCI generic platform driver
[ 1.756570] ohci_hcd: USB 1.1 'Open' Host Controller (OHCI) Driver
[ 1.756573] ohci-pci: OHCI PCI platform driver
[ 1.756584] ohci-platform: OHCI generic platform driver
[ 1.756592] uhci_hcd: USB Universal Host Controller Interface driver
[ 1.756714] uhci_hcd 0000:00:1a.0: UHCI Host Controller
[ 1.756719] uhci_hcd 0000:00:1a.0: new USB bus registered, assigned bus number 3
[ 1.756724] uhci_hcd 0000:00:1a.0: detected 2 ports
[ 1.756746] uhci_hcd 0000:00:1a.0: irq 16, io base 0x00009400
[ 1.756782] usb usb3: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.756783] usb usb3: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.756785] usb usb3: Product: UHCI Host Controller
[ 1.756786] usb usb3: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.756787] usb usb3: SerialNumber: 0000:00:1a.0
[ 1.757042] hub 3-0:1.0: USB hub found
[ 1.757053] hub 3-0:1.0: 2 ports detected
[ 1.757277] uhci_hcd 0000:00:1a.1: UHCI Host Controller
[ 1.757281] uhci_hcd 0000:00:1a.1: new USB bus registered, assigned bus number 4
[ 1.757286] uhci_hcd 0000:00:1a.1: detected 2 ports
[ 1.757313] uhci_hcd 0000:00:1a.1: irq 21, io base 0x00009480
[ 1.757349] usb usb4: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.757350] usb usb4: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.757351] usb usb4: Product: UHCI Host Controller
[ 1.757353] usb usb4: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.757354] usb usb4: SerialNumber: 0000:00:1a.1
[ 1.757596] hub 4-0:1.0: USB hub found
[ 1.757606] hub 4-0:1.0: 2 ports detected
[ 1.757827] uhci_hcd 0000:00:1a.2: UHCI Host Controller
[ 1.757831] uhci_hcd 0000:00:1a.2: new USB bus registered, assigned bus number 5
[ 1.757836] uhci_hcd 0000:00:1a.2: detected 2 ports
[ 1.757857] uhci_hcd 0000:00:1a.2: irq 19, io base 0x00009800
[ 1.757895] usb usb5: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.757897] usb usb5: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.757898] usb usb5: Product: UHCI Host Controller
[ 1.757899] usb usb5: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.757900] usb usb5: SerialNumber: 0000:00:1a.2
[ 1.758151] hub 5-0:1.0: USB hub found
[ 1.758163] hub 5-0:1.0: 2 ports detected
[ 1.758377] uhci_hcd 0000:00:1d.0: UHCI Host Controller
[ 1.758386] uhci_hcd 0000:00:1d.0: new USB bus registered, assigned bus number 6
[ 1.758391] uhci_hcd 0000:00:1d.0: detected 2 ports
[ 1.758411] uhci_hcd 0000:00:1d.0: irq 23, io base 0x00009880
[ 1.758452] usb usb6: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.758453] usb usb6: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.758454] usb usb6: Product: UHCI Host Controller
[ 1.758456] usb usb6: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.758457] usb usb6: SerialNumber: 0000:00:1d.0
[ 1.758708] hub 6-0:1.0: USB hub found
[ 1.758719] hub 6-0:1.0: 2 ports detected
[ 1.758934] uhci_hcd 0000:00:1d.1: UHCI Host Controller
[ 1.758939] uhci_hcd 0000:00:1d.1: new USB bus registered, assigned bus number 7
[ 1.758944] uhci_hcd 0000:00:1d.1: detected 2 ports
[ 1.758960] uhci_hcd 0000:00:1d.1: irq 19, io base 0x00009c00
[ 1.758996] usb usb7: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.758998] usb usb7: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.758999] usb usb7: Product: UHCI Host Controller
[ 1.759000] usb usb7: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.759001] usb usb7: SerialNumber: 0000:00:1d.1
[ 1.759106] hub 7-0:1.0: USB hub found
[ 1.759111] hub 7-0:1.0: 2 ports detected
[ 1.759306] uhci_hcd 0000:00:1d.2: UHCI Host Controller
[ 1.759310] uhci_hcd 0000:00:1d.2: new USB bus registered, assigned bus number 8
[ 1.759315] uhci_hcd 0000:00:1d.2: detected 2 ports
[ 1.759332] uhci_hcd 0000:00:1d.2: irq 18, io base 0x0000a000
[ 1.759373] usb usb8: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.759374] usb usb8: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.759375] usb usb8: Product: UHCI Host Controller
[ 1.759376] usb usb8: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.759378] usb usb8: SerialNumber: 0000:00:1d.2
[ 1.759500] hub 8-0:1.0: USB hub found
[ 1.759505] hub 8-0:1.0: 2 ports detected
[ 1.759627] i8042: PNP: No PS/2 controller found.
[ 1.759628] i8042: Probing ports directly.
[ 1.762394] serio: i8042 KBD port at 0x60,0x64 irq 1
[ 1.762398] serio: i8042 AUX port at 0x60,0x64 irq 12
[ 1.762543] mousedev: PS/2 mouse device common for all mice
[ 1.762873] rtc_cmos 00:01: RTC can wake from S4
[ 1.763041] rtc_cmos 00:01: registered as rtc0
[ 1.763058] rtc_cmos 00:01: alarms up to one month, y3k, 114 bytes nvram, hpet irqs
[ 1.763063] i2c /dev entries driver
[ 1.763104] device-mapper: uevent: version 1.0.3
[ 1.763165] device-mapper: ioctl: 4.39.0-ioctl (2018-04-03) initialised: dm-devel@redhat.com
[ 1.764801] ledtrig-cpu: registered to indicate activity on CPUs
[ 1.765699] NET: Registered protocol family 10
[ 1.770650] Segment Routing with IPv6
[ 1.770680] NET: Registered protocol family 17
[ 1.770805] Key type dns_resolver registered
[ 1.774461] RAS: Correctable Errors collector initialized.
[ 1.774532] microcode: sig=0x206c2, pf=0x1, revision=0x14
[ 1.775780] microcode: Microcode Update Driver: v2.2.
[ 1.775794] sched_clock: Marking stable (1775770135, 0)->(1957017621, -181247486)
[ 1.791805] registered taskstats version 1
[ 1.791826] Loading compiled-in X.509 certificates
[ 1.794790] Loaded X.509 cert 'Build time autogenerated kernel key: 8a422d2124cd616d9582218b11710484582c209e'
[ 1.794828] zswap: loaded using pool lzo/zbud
[ 1.810682] Key type big_key registered
[ 1.810687] Key type trusted registered
[ 1.812759] Key type encrypted registered
[ 1.812764] AppArmor: AppArmor sha1 policy hashing enabled
[ 1.812767] ima: No TPM chip found, activating TPM-bypass! (rc=-19)
[ 1.812774] ima: Allocated hash algorithm: sha1
[ 1.812804] evm: HMAC attrs: 0x1
[ 1.813327] Magic number: 2:641:930
[ 1.813329] hash matches drivers/base/power/main.c:1812
[ 1.813438] memory memory357: hash matches
[ 1.814535] rtc_cmos 00:01: setting system clock to 2018-05-24 09:55:21 UTC (1527155721)
[ 1.826042] Freeing unused kernel memory: 2428K
[ 1.844110] Write protecting the kernel read-only data: 20480k
[ 1.850306] Freeing unused kernel memory: 2008K
[ 1.856099] Freeing unused kernel memory: 1812K
[ 1.862087] nvme0n1: p1 p2 p3
[ 1.867009] x86/mm: Checked W+X mappings: passed, no W+X pages found.
[ 1.867009] x86/mm: Checking user space page tables
[ 1.877499] x86/mm: Checked W+X mappings: passed, no W+X pages found.
[ 1.995610] e1000e: Intel(R) PRO/1000 Network Driver - 3.2.6-k
[ 1.995611] e1000e: Copyright(c) 1999 - 2015 Intel Corporation.
[ 1.995827] e1000e 0000:03:00.0: Interrupt Throttling Rate (ints/sec) set to dynamic conservative mode
[ 2.006852] ahci 0000:00:1f.2: version 3.0
[ 2.007057] ahci 0000:00:1f.2: SSS flag set, parallel bus scan disabled
[ 2.007094] ahci 0000:00:1f.2: AHCI 0001.0200 32 slots 6 ports 3 Gbps 0x3f impl SATA mode
[ 2.007097] ahci 0000:00:1f.2: flags: 64bit ncq sntf stag pm led clo pio slum part ccc ems sxs
[ 2.012145] tsc: Refined TSC clocksource calibration: 3066.777 MHz
[ 2.012406] clocksource: tsc: mask: 0xffffffffffffffff max_cycles: 0x2c34af8fe07, max_idle_ns: 440795322837 ns
[ 2.012554] clocksource: Switched to clocksource tsc
[ 2.054868] e1000e 0000:03:00.0 0000:03:00.0 (uninitialized): registered PHC clock
[ 2.064838] scsi host0: ahci
[ 2.065155] scsi host1: ahci
[ 2.065396] scsi host2: ahci
[ 2.065653] scsi host3: ahci
[ 2.065759] scsi host4: ahci
[ 2.065949] scsi host5: ahci
[ 2.066001] ata1: SATA max UDMA/133 abar m2048@0xf7bfc000 port 0xf7bfc100 irq 36
[ 2.066002] ata2: SATA max UDMA/133 abar m2048@0xf7bfc000 port 0xf7bfc180 irq 36
[ 2.066004] ata3: SATA max UDMA/133 abar m2048@0xf7bfc000 port 0xf7bfc200 irq 36
[ 2.066005] ata4: SATA max UDMA/133 abar m2048@0xf7bfc000 port 0xf7bfc280 irq 36
[ 2.066007] ata5: SATA max UDMA/133 abar m2048@0xf7bfc000 port 0xf7bfc300 irq 36
[ 2.066008] ata6: SATA max UDMA/133 abar m2048@0xf7bfc000 port 0xf7bfc380 irq 36
[ 2.114071] e1000e 0000:03:00.0 eth0: (PCI Express:2.5GT/s:Width x1) 00:e0:81:d6:04:63
[ 2.114073] e1000e 0000:03:00.0 eth0: Intel(R) PRO/1000 Network Connection
[ 2.114157] e1000e 0000:03:00.0 eth0: MAC: 3, PHY: 8, PBA No: FFFFFF-0FF
[ 2.114365] e1000e 0000:02:00.0: Interrupt Throttling Rate (ints/sec) set to dynamic conservative mode
[ 2.120409] [drm] amdgpu kernel modesetting enabled.
[ 2.129948] AMD IOMMUv2 driver by Joerg Roedel <jroedel@suse.de>
[ 2.129949] AMD IOMMUv2 functionality not available on this system
[ 2.173867] e1000e 0000:02:00.0 0000:02:00.0 (uninitialized): registered PHC clock
[ 2.174288] CRAT table not found
[ 2.174291] Virtual CRAT table created for CPU
[ 2.174293] Parsing CRAT table with 2 nodes
[ 2.174296] Creating topology SYSFS entries
[ 2.174329] Topology: Add CPU node
[ 2.174330] Finished initializing topology
[ 2.174438] kfd kfd: Initialized module
[ 2.175486] checking generic (ef000000 500000) vs hw (fed0000000 10000000)
[ 2.175553] amdgpu 0000:06:00.0: enabling device (0000 -> 0003)
[ 2.175874] [drm] initializing kernel modesetting (POLARIS11 0x1002:0x67FF 0x1DA2:0xE367 0xFF).
[ 2.175885] [drm] register mmio base: 0xF7E80000
[ 2.175886] [drm] register mmio size: 262144
[ 2.175896] [drm] probing gen 2 caps for device 8086:340e = 393042/0
[ 2.175898] [drm] probing mlw for device 8086:340e = 393042
[ 2.175900] [drm] add ip block number 0 <vi_common>
[ 2.175901] [drm] add ip block number 1 <gmc_v8_0>
[ 2.175902] [drm] add ip block number 2 <tonga_ih>
[ 2.175903] [drm] add ip block number 3 <powerplay>
[ 2.175905] [drm] add ip block number 4 <dm>
[ 2.175906] [drm] add ip block number 5 <gfx_v8_0>
[ 2.175907] [drm] add ip block number 6 <sdma_v3_0>
[ 2.175908] [drm] add ip block number 7 <uvd_v6_0>
[ 2.175909] [drm] add ip block number 8 <vce_v3_0>
[ 2.175914] kfd kfd: skipped device 1002:67ff, PCI rejects atomics
[ 2.175926] [drm] UVD is enabled in VM mode
[ 2.175927] [drm] UVD ENC is enabled in VM mode
[ 2.175930] [drm] VCE enabled in VM mode
[ 2.232106] usb 6-1: new low-speed USB device number 2 using uhci_hcd
[ 2.237003] e1000e 0000:02:00.0 eth1: (PCI Express:2.5GT/s:Width x1) 00:e0:81:d6:04:64
[ 2.237006] e1000e 0000:02:00.0 eth1: Intel(R) PRO/1000 Network Connection
[ 2.237117] e1000e 0000:02:00.0 eth1: MAC: 3, PHY: 8, PBA No: FFFFFF-0FF
[ 2.240637] e1000e 0000:03:00.0 enp3s0: renamed from eth0
[ 2.379066] ata1: SATA link up 3.0 Gbps (SStatus 123 SControl 300)
[ 2.380813] ata1.00: supports DRM functions and may not be fully accessible
[ 2.381419] ata1.00: NCQ Send/Recv Log not supported
[ 2.381420] ata1.00: ATA-9: Samsung SSD 850 EVO 120GB, EMT01B6Q, max UDMA/133
[ 2.381422] ata1.00: 234441648 sectors, multi 1: LBA48 NCQ (depth 31/32), AA
[ 2.383069] ata1.00: supports DRM functions and may not be fully accessible
[ 2.383605] ata1.00: NCQ Send/Recv Log not supported
[ 2.384792] ata1.00: configured for UDMA/133
[ 2.385095] scsi 0:0:0:0: Direct-Access ATA Samsung SSD 850 1B6Q PQ: 0 ANSI: 5
[ 2.385494] sd 0:0:0:0: Attached scsi generic sg0 type 0
[ 2.385496] sd 0:0:0:0: [sda] 234441648 512-byte logical blocks: (120 GB/112 GiB)
[ 2.385504] sd 0:0:0:0: [sda] Write Protect is off
[ 2.385506] sd 0:0:0:0: [sda] Mode Sense: 00 3a 00 00
[ 2.385517] sd 0:0:0:0: [sda] Write cache: enabled, read cache: enabled, doesn't support DPO or FUA
[ 2.386210] sda: sda1 sda2 < sda5 >
[ 2.387067] sd 0:0:0:0: [sda] supports TCG Opal
[ 2.387069] sd 0:0:0:0: [sda] Attached SCSI disk
[ 2.399155] ATOM BIOS: 113-367BF-U41
[ 2.399166] [drm] GPU posting now...
[ 2.432110] usb 6-1: New USB device found, idVendor=046d, idProduct=c077, bcdDevice=72.00
[ 2.432112] usb 6-1: New USB device strings: Mfr=1, Product=2, SerialNumber=0
[ 2.432113] usb 6-1: Product: USB Optical Mouse
[ 2.432115] usb 6-1: Manufacturer: Logitech
[ 2.445550] hidraw: raw HID events driver (C) Jiri Kosina
[ 2.466187] usbcore: registered new interface driver usbhid
[ 2.466187] usbhid: USB HID core driver
[ 2.476240] input: Logitech USB Optical Mouse as /devices/pci0000:00/0000:00:1d.0/usb6/6-1/6-1:1.0/0003:046D:C077.0001/input/input5
[ 2.476611] hid-generic 0003:046D:C077.0001: input,hidraw0: USB HID v1.11 Mouse [Logitech USB Optical Mouse] on usb-0000:00:1d.0-1/input0
[ 2.508282] e1000e 0000:02:00.0 enp2s0: renamed from eth1
[ 2.511967] [drm] vm size is 64 GB, 2 levels, block size is 10-bit, fragment size is 9-bit
[ 2.512066] amdgpu 0000:06:00.0: BAR 2: releasing [mem 0xfecfe00000-0xfecfffffff 64bit pref]
[ 2.512068] amdgpu 0000:06:00.0: BAR 0: releasing [mem 0xfed0000000-0xfedfffffff 64bit pref]
[ 2.512083] pcieport 0000:00:07.0: BAR 15: releasing [mem 0xfecfe00000-0xfedfffffff 64bit pref]
[ 2.512096] pcieport 0000:00:07.0: BAR 15: no space for [mem size 0x180000000 64bit pref]
[ 2.512098] pcieport 0000:00:07.0: BAR 15: failed to assign [mem size 0x180000000 64bit pref]
[ 2.512100] amdgpu 0000:06:00.0: BAR 0: no space for [mem size 0x100000000 64bit pref]
[ 2.512102] amdgpu 0000:06:00.0: BAR 0: failed to assign [mem size 0x100000000 64bit pref]
[ 2.512104] amdgpu 0000:06:00.0: BAR 2: no space for [mem size 0x00200000 64bit pref]
[ 2.512105] amdgpu 0000:06:00.0: BAR 2: failed to assign [mem size 0x00200000 64bit pref]
[ 2.512107] pcieport 0000:00:07.0: PCI bridge to [bus 06]
[ 2.512109] pcieport 0000:00:07.0: bridge window [io 0xd000-0xdfff]
[ 2.512112] pcieport 0000:00:07.0: bridge window [mem 0xf7e00000-0xf7efffff]
[ 2.512117] pcieport 0000:00:07.0: PCI bridge to [bus 06]
[ 2.512119] pcieport 0000:00:07.0: bridge window [io 0xd000-0xdfff]
[ 2.512122] pcieport 0000:00:07.0: bridge window [mem 0xf7e00000-0xf7efffff]
[ 2.512124] pcieport 0000:00:07.0: bridge window [mem 0xfecfe00000-0xfedfffffff 64bit pref]
[ 2.512132] [drm] Not enough PCI address space for a large BAR.
[ 2.512134] amdgpu 0000:06:00.0: BAR 0: assigned [mem 0xfed0000000-0xfedfffffff 64bit pref]
[ 2.512141] amdgpu 0000:06:00.0: BAR 2: assigned [mem 0xfecfe00000-0xfecfffffff 64bit pref]
[ 2.512155] amdgpu 0000:06:00.0: VRAM: 4096M 0x000000F400000000 - 0x000000F4FFFFFFFF (4096M used)
[ 2.512156] amdgpu 0000:06:00.0: GTT: 256M 0x0000000000000000 - 0x000000000FFFFFFF
[ 2.512158] [drm] Detected VRAM RAM=4096M, BAR=256M
[ 2.512159] [drm] RAM width 128bits GDDR5
[ 2.512358] [TTM] Zone kernel: Available graphics memory: 24721732 kiB
[ 2.512359] [TTM] Zone dma32: Available graphics memory: 2097152 kiB
[ 2.512359] [TTM] Initializing pool allocator
[ 2.512363] [TTM] Initializing DMA pool allocator
[ 2.512392] [drm] amdgpu: 4096M of VRAM memory ready
[ 2.512396] [drm] amdgpu: 4096M of GTT memory ready.
[ 2.512405] [drm] GART: num cpu pages 65536, num gpu pages 65536
[ 2.512458] [drm] PCIE GART of 256M enabled (table at 0x000000F400040000).
[ 2.512583] [drm] Chained IB support enabled!
[ 2.514925] [drm] Found UVD firmware Version: 1.130 Family ID: 16
[ 2.516258] [drm] Found VCE firmware Version: 52.4 Binary ID: 3
[ 2.581328] amdgpu: [powerplay]
failed to send message 309 ret is 254
[ 2.581344] amdgpu: [powerplay]
failed to send pre message 14e ret is 254
[ 2.590941] [drm] DM_PPLIB: values for Engine clock
[ 2.590942] [drm] DM_PPLIB: 21400
[ 2.590942] [drm] DM_PPLIB: 33500
[ 2.590943] [drm] DM_PPLIB: 50300
[ 2.590943] [drm] DM_PPLIB: 69700
[ 2.590944] [drm] DM_PPLIB: 87400
[ 2.590944] [drm] DM_PPLIB: 101900
[ 2.590944] [drm] DM_PPLIB: 104300
[ 2.590945] [drm] DM_PPLIB: 107100
[ 2.590945] [drm] DM_PPLIB: Validation clocks:
[ 2.590946] [drm] DM_PPLIB: engine_max_clock: 107100
[ 2.590946] [drm] DM_PPLIB: memory_max_clock: 150000
[ 2.590947] [drm] DM_PPLIB: level : 0
[ 2.590948] [drm] DM_PPLIB: values for Memory clock
[ 2.590948] [drm] DM_PPLIB: 30000
[ 2.590949] [drm] DM_PPLIB: 62500
[ 2.590949] [drm] DM_PPLIB: 150000
[ 2.590950] [drm] DM_PPLIB: Validation clocks:
[ 2.590950] [drm] DM_PPLIB: engine_max_clock: 107100
[ 2.590950] [drm] DM_PPLIB: memory_max_clock: 150000
[ 2.590951] [drm] DM_PPLIB: level : 0
[ 2.591835] [drm] Display Core initialized with v3.1.38!
[ 2.592452] [drm] Supports vblank timestamp caching Rev 2 (21.10.2013).
[ 2.592453] [drm] Driver supports precise vblank timestamp query.
[ 2.622295] [drm] UVD and UVD ENC initialized successfully.
[ 2.699078] ata2: SATA link up 3.0 Gbps (SStatus 123 SControl 300)
[ 2.722223] [drm] VCE initialized successfully.
[ 2.764996] ata2.00: ATA-8: TOSHIBA MG03ACA200, FL1A, max UDMA/100
[ 2.764999] ata2.00: 3907029168 sectors, multi 16: LBA48 NCQ (depth 31/32), AA
[ 2.766282] ata2.00: configured for UDMA/100
[ 2.766715] scsi 1:0:0:0: Direct-Access ATA TOSHIBA MG03ACA2 FL1A PQ: 0 ANSI: 5
[ 2.767165] sd 1:0:0:0: [sdb] 3907029168 512-byte logical blocks: (2.00 TB/1.82 TiB)
[ 2.767176] sd 1:0:0:0: [sdb] Write Protect is off
[ 2.767178] sd 1:0:0:0: [sdb] Mode Sense: 00 3a 00 00
[ 2.767189] sd 1:0:0:0: [sdb] Write cache: enabled, read cache: enabled, doesn't support DPO or FUA
[ 2.767230] sd 1:0:0:0: Attached scsi generic sg1 type 0
[ 2.856084] usb 2-2: new high-speed USB device number 3 using ehci-pci
[ 2.948323] sdb: sdb1 sdb2
[ 2.948954] sd 1:0:0:0: [sdb] Attached SCSI disk
[ 3.014272] usb 2-2: New USB device found, idVendor=18a5, idProduct=022e, bcdDevice= 1.00
[ 3.014276] usb 2-2: New USB device strings: Mfr=10, Product=11, SerialNumber=3
[ 3.014278] usb 2-2: Product: Portable USB 3.0 Drive
[ 3.014280] usb 2-2: Manufacturer: Verbatim
[ 3.014282] usb 2-2: SerialNumber: 20051C075244
[ 3.083381] ata3: SATA link down (SStatus 0 SControl 300)
[ 3.237269] [drm] Cannot find any crtc or sizes
[ 3.239297] [drm] Initialized amdgpu 3.25.0 20150101 for 0000:06:00.0 on minor 0
[ 3.276098] usb 7-2: new low-speed USB device number 2 using uhci_hcd
[ 3.399731] ata4: SATA link up 1.5 Gbps (SStatus 113 SControl 300)
[ 3.402282] ata4.00: ATAPI: TSSTcorp CDDVDW SH-224FB, SB00, max UDMA/100
[ 3.405617] ata4.00: configured for UDMA/100
[ 3.407465] scsi 3:0:0:0: CD-ROM TSSTcorp CDDVDW SH-224FB SB00 PQ: 0 ANSI: 5
[ 3.468499] sr 3:0:0:0: [sr0] scsi3-mmc drive: 48x/48x writer dvd-ram cd/rw xa/form2 cdda tray
[ 3.468501] cdrom: Uniform CD-ROM driver Revision: 3.20
[ 3.468663] sr 3:0:0:0: Attached scsi CD-ROM sr0
[ 3.468791] sr 3:0:0:0: Attached scsi generic sg2 type 5
[ 3.571158] usb 7-2: New USB device found, idVendor=04d9, idProduct=1702, bcdDevice= 4.06
[ 3.571161] usb 7-2: New USB device strings: Mfr=1, Product=2, SerialNumber=0
[ 3.571164] usb 7-2: Product: USB Keyboard
[ 3.571166] usb 7-2: Manufacturer:
[ 3.631419] input: USB Keyboard as /devices/pci0000:00/0000:00:1d.1/usb7/7-2/7-2:1.0/0003:04D9:1702.0002/input/input6
[ 3.688463] hid-generic 0003:04D9:1702.0002: input,hidraw1: USB HID v1.10 Keyboard [ USB Keyboard] on usb-0000:00:1d.1-2/input0
[ 3.770367] input: USB Keyboard as /devices/pci0000:00/0000:00:1d.1/usb7/7-2/7-2:1.1/0003:04D9:1702.0003/input/input7
[ 3.783593] ata5: SATA link up 1.5 Gbps (SStatus 113 SControl 300)
[ 3.784590] ata5.00: ATAPI: QUANTUM DLT-V4, 0A00, max UDMA/133
[ 3.785753] ata5.00: configured for UDMA/133
[ 3.788079] scsi 4:0:0:0: Sequential-Access QUANTUM DLT-V4 0A00 PQ: 0 ANSI: 2
[ 3.788394] scsi 4:0:0:0: Attached scsi generic sg3 type 1
[ 3.828458] hid-generic 0003:04D9:1702.0003: input,hidraw2: USB HID v1.10 Device [ USB Keyboard] on usb-0000:00:1d.1-2/input1
[ 3.900083] usb 2-5: new high-speed USB device number 5 using ehci-pci
[ 4.073774] usb 2-5: New USB device found, idVendor=046b, idProduct=ff01, bcdDevice= 1.00
[ 4.073777] usb 2-5: New USB device strings: Mfr=1, Product=2, SerialNumber=3
[ 4.073779] usb 2-5: Product: Generic Hub
[ 4.073782] usb 2-5: Manufacturer: American Megatrends Inc.
[ 4.073784] usb 2-5: SerialNumber: serial
[ 4.074548] hub 2-5:1.0: USB hub found
[ 4.074811] hub 2-5:1.0: 3 ports detected
[ 4.103458] ata6: SATA link down (SStatus 0 SControl 300)
[ 4.116876] random: fast init done
[ 4.118963] st: Version 20160209, fixed bufsize 32768, s/g segs 256
[ 4.119311] st 4:0:0:0: Attached scsi tape st0
[ 4.119313] st 4:0:0:0: st0: try direct i/o: yes (alignment 512 B)
[ 4.130596] osst :I: Tape driver with OnStream support version 0.99.4
osst :I: $Id: osst.c,v 1.73 2005/01/01 21:13:34 wriede Exp $
[ 4.360039] usb 2-5.1: new low-speed USB device number 6 using ehci-pci
[ 4.383637] usb-storage 2-2:1.0: USB Mass Storage device detected
[ 4.383993] scsi host6: usb-storage 2-2:1.0
[ 4.384067] usbcore: registered new interface driver usb-storage
[ 4.393981] usbcore: registered new interface driver uas
[ 4.482175] usb 2-5.1: New USB device found, idVendor=046b, idProduct=ff10, bcdDevice= 1.00
[ 4.482179] usb 2-5.1: New USB device strings: Mfr=1, Product=2, SerialNumber=3
[ 4.482181] usb 2-5.1: Product: Virtual Keyboard and Mouse
[ 4.482183] usb 2-5.1: Manufacturer: American Megatrends Inc.
[ 4.482186] usb 2-5.1: SerialNumber: serial
[ 4.484526] input: American Megatrends Inc. Virtual Keyboard and Mouse as /devices/pci0000:00/0000:00:1d.7/usb2/2-5/2-5.1/2-5.1:1.0/0003:046B:FF10.0004/input/input8
[ 4.484898] hid-generic 0003:046B:FF10.0004: input,hidraw3: USB HID v1.10 Keyboard [American Megatrends Inc. Virtual Keyboard and Mouse] on usb-0000:00:1d.7-5.1/input0
[ 4.486180] input: American Megatrends Inc. Virtual Keyboard and Mouse as /devices/pci0000:00/0000:00:1d.7/usb2/2-5/2-5.1/2-5.1:1.1/0003:046B:FF10.0005/input/input9
[ 4.486520] hid-generic 0003:046B:FF10.0005: input,hidraw4: USB HID v1.10 Mouse [American Megatrends Inc. Virtual Keyboard and Mouse] on usb-0000:00:1d.7-5.1/input1
[ 5.405266] scsi 6:0:0:0: Direct-Access Hitachi HTS543216L9A300 0100 PQ: 0 ANSI: 2 CCS
[ 5.405880] sd 6:0:0:0: Attached scsi generic sg4 type 0
[ 5.406379] sd 6:0:0:0: [sdc] 312581808 512-byte logical blocks: (160 GB/149 GiB)
[ 5.407532] sd 6:0:0:0: [sdc] Write Protect is off
[ 5.407535] sd 6:0:0:0: [sdc] Mode Sense: 28 00 00 00
[ 5.408670] sd 6:0:0:0: [sdc] No Caching mode page found
[ 5.410821] sd 6:0:0:0: [sdc] Assuming drive cache: write through
[ 5.467116] sdc: sdc1 sdc2 < sdc5 sdc6 >
[ 5.471288] sd 6:0:0:0: [sdc] Attached SCSI disk
[ 36.692931] random: crng init done
[ 38.931854] EXT4-fs (sdc1): mounted filesystem with ordered data mode. Opts: (null)
[ 40.963213] systemd[1]: systemd 237 running in system mode. (+PAM +AUDIT +SELINUX +IMA +APPARMOR +SMACK +SYSVINIT +UTMP +LIBCRYPTSETUP +GCRYPT +GNUTLS +ACL +XZ +LZ4 +SECCOMP +BLKID +ELFUTILS +KMOD -IDN2 +IDN -PCRE2 default-hierarchy=hybrid)
[ 40.985595] systemd[1]: Detected architecture x86-64.
[ 41.232201] systemd[1]: Set hostname to <lpnm-empty>.
[ 43.969619] systemd[1]: Reached target User and Group Name Lookups.
[ 43.969679] systemd[1]: Reached target Remote File Systems.
[ 43.969730] systemd[1]: Started Forward Password Requests to Wall Directory Watch.
[ 43.969892] systemd[1]: Set up automount Arbitrary Executable File Formats File System Automount Point.
[ 43.970057] systemd[1]: Created slice User and Session Slice.
[ 43.970190] systemd[1]: Created slice System Slice.
[ 43.970260] systemd[1]: Listening on fsck to fsckd communication Socket.
[ 44.902065] EXT4-fs (sdc1): re-mounted. Opts: errors=remount-ro
[ 46.964498] lp: driver loaded but no devices found
[ 47.741797] systemd-journald[509]: Received request to flush runtime journal from PID 1
[ 47.764029] ppdev: user-space parallel port driver
[ 58.306937] systemd-journald[509]: File /var/log/journal/40d705ecb985487d87725bd5ed268b7c/system.journal corrupted or uncleanly shut down, renaming and replacing.
[ 59.971310] shpchp: Standard Hot Plug PCI Controller Driver version: 0.4
[ 60.036483] ipmi message handler version 39.2
[ 60.419060] EDAC MC1: Giving out device to module i7core_edac.c controller i7 core #1: DEV 0000:fe:03.0 (INTERRUPT)
[ 60.419080] EDAC PCI0: Giving out device to module i7core_edac controller EDAC PCI controller: DEV 0000:fe:03.0 (POLLED)
[ 60.419311] EDAC MC0: Giving out device to module i7core_edac.c controller i7 core #0: DEV 0000:ff:03.0 (INTERRUPT)
[ 60.419326] EDAC PCI1: Giving out device to module i7core_edac controller EDAC PCI controller: DEV 0000:ff:03.0 (POLLED)
[ 60.419336] EDAC i7core: Driver loaded, 2 memory controller(s) found.
[ 60.425609] ipmi device interface
[ 60.531003] i5500_temp 0000:00:14.3: Sensor seems to be disabled
[ 60.531016] i5500_temp 0000:80:14.3: Sensor seems to be disabled
[ 61.504000] IPMI System Interface driver.
[ 61.504029] ipmi_si dmi-ipmi-si.0: ipmi_platform: probing via SMBIOS
[ 61.504031] ipmi_si: SMBIOS: io 0xca8 regsize 1 spacing 4 irq 0
[ 61.504031] ipmi_si: Adding SMBIOS-specified kcs state machine
[ 61.504097] ipmi_si: Trying SMBIOS-specified kcs state machine at i/o address 0xca8, slave address 0x20, irq 0
[ 61.677226] cryptd: max_cpu_qlen set to 1000
[ 61.864975] ipmi_si dmi-ipmi-si.0: Found new BMC (man_id: 0x0019fd, prod_id: 0x1b71, dev_id: 0x20)
[ 61.896542] ipmi_si dmi-ipmi-si.0: IPMI kcs interface initialized
[ 62.928351] gpio_ich: GPIO from 451 to 511 on gpio_ich
[ 63.518814] SSE version of gcm_enc/dec engaged.
[ 63.862776] snd_hda_intel 0000:08:00.1: Disabling MSI
[ 63.862784] snd_hda_intel 0000:08:00.1: Handle vga_switcheroo audio client
[ 63.862956] snd_hda_intel 0000:06:00.1: Handle vga_switcheroo audio client
[ 63.862958] snd_hda_intel 0000:06:00.1: Force to non-snoop mode
[ 64.073102] input: HDA ATI HDMI HDMI/DP,pcm=3 as /devices/pci0000:00/0000:00:07.0/0000:06:00.1/sound/card2/input10
[ 64.073165] input: HDA ATI HDMI HDMI/DP,pcm=7 as /devices/pci0000:00/0000:00:07.0/0000:06:00.1/sound/card2/input11
[ 64.073212] input: HDA ATI HDMI HDMI/DP,pcm=8 as /devices/pci0000:00/0000:00:07.0/0000:06:00.1/sound/card2/input12
[ 64.073262] input: HDA ATI HDMI HDMI/DP,pcm=9 as /devices/pci0000:00/0000:00:07.0/0000:06:00.1/sound/card2/input13
[ 64.073306] input: HDA ATI HDMI HDMI/DP,pcm=10 as /devices/pci0000:00/0000:00:07.0/0000:06:00.1/sound/card2/input14
[ 64.419107] snd_hda_codec_realtek hdaudioC0D0: ALC262: SKU not ready 0x411111f0
[ 64.419785] snd_hda_codec_realtek hdaudioC0D0: ignore pin 0x1b with mismatching assoc# 0x2 vs 0x1
[ 64.420037] snd_hda_codec_realtek hdaudioC0D0: autoconfig for ALC262: line_outs=1 (0x14/0x0/0x0/0x0/0x0) type:line
[ 64.420039] snd_hda_codec_realtek hdaudioC0D0: speaker_outs=0 (0x0/0x0/0x0/0x0/0x0)
[ 64.420041] snd_hda_codec_realtek hdaudioC0D0: hp_outs=0 (0x0/0x0/0x0/0x0/0x0)
[ 64.420042] snd_hda_codec_realtek hdaudioC0D0: mono: mono_out=0x0
[ 64.420043] snd_hda_codec_realtek hdaudioC0D0: dig-out=0x1e/0x0
[ 64.420044] snd_hda_codec_realtek hdaudioC0D0: inputs:
[ 64.420046] snd_hda_codec_realtek hdaudioC0D0: Rear Mic=0x18
[ 64.420047] snd_hda_codec_realtek hdaudioC0D0: Front Mic=0x19
[ 64.420049] snd_hda_codec_realtek hdaudioC0D0: Line=0x1a
[ 64.420050] snd_hda_codec_realtek hdaudioC0D0: CD=0x1c
[ 64.420051] snd_hda_codec_realtek hdaudioC0D0: dig-in=0x1f
[ 64.432897] input: HDA Intel Rear Mic as /devices/pci0000:00/0000:00:1b.0/sound/card0/input15
[ 64.433007] input: HDA Intel Front Mic as /devices/pci0000:00/0000:00:1b.0/sound/card0/input16
[ 64.433081] input: HDA Intel Line as /devices/pci0000:00/0000:00:1b.0/sound/card0/input17
[ 64.433122] input: HDA Intel Line Out as /devices/pci0000:00/0000:00:1b.0/sound/card0/input18
[ 64.669326] input: HDA NVidia HDMI/DP,pcm=3 as /devices/pci0000:00/0000:00:03.0/0000:08:00.1/sound/card1/input19
[ 64.669471] input: HDA NVidia HDMI/DP,pcm=7 as /devices/pci0000:00/0000:00:03.0/0000:08:00.1/sound/card1/input20
[ 64.669619] input: HDA NVidia HDMI/DP,pcm=8 as /devices/pci0000:00/0000:00:03.0/0000:08:00.1/sound/card1/input21
[ 64.749159] kvm: VM_EXIT_LOAD_IA32_PERF_GLOBAL_CTRL does not work properly. Using workaround
[ 68.401189] Adding 2440188k swap on /dev/sdc5. Priority:-2 extents:1 across:2440188k FS
[ 68.664728] EXT4-fs (sdc6): mounted filesystem with ordered data mode. Opts: (null)
[ 69.373281] audit: type=1400 audit(1527155789.055:2): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/lib/lightdm/lightdm-guest-session" pid=1045 comm="apparmor_parser"
[ 69.373287] audit: type=1400 audit(1527155789.055:3): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/lib/lightdm/lightdm-guest-session//chromium" pid=1045 comm="apparmor_parser"
[ 69.381328] audit: type=1400 audit(1527155789.063:4): apparmor="STATUS" operation="profile_load" profile="unconfined" name="libreoffice-senddoc" pid=1052 comm="apparmor_parser"
[ 69.381335] audit: type=1400 audit(1527155789.063:5): apparmor="STATUS" operation="profile_load" profile="unconfined" name="libreoffice-senddoc//sanitized_helper" pid=1052 comm="apparmor_parser"
[ 69.383096] audit: type=1400 audit(1527155789.063:6): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/sbin/tcpdump" pid=1060 comm="apparmor_parser"
[ 69.384022] audit: type=1400 audit(1527155789.063:7): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/sbin/cups-browsed" pid=1056 comm="apparmor_parser"
[ 69.405343] audit: type=1400 audit(1527155789.087:8): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/snap/core/4650/usr/lib/snapd/snap-confine" pid=1047 comm="apparmor_parser"
[ 69.405350] audit: type=1400 audit(1527155789.087:9): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/snap/core/4650/usr/lib/snapd/snap-confine//mount-namespace-capture-helper" pid=1047 comm="apparmor_parser"
[ 69.408403] audit: type=1400 audit(1527155789.091:10): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/sbin/dhclient" pid=1046 comm="apparmor_parser"
[ 69.408409] audit: type=1400 audit(1527155789.091:11): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/lib/NetworkManager/nm-dhcp-client.action" pid=1046 comm="apparmor_parser"
[ 137.547656] checking generic (ef000000 500000) vs hw (fef0000000 10000000)
[ 137.547658] checking generic (ef000000 500000) vs hw (feee000000 2000000)
[ 137.547706] nouveau 0000:08:00.0: NVIDIA GP107 (137000a1)
[ 137.663750] nouveau 0000:08:00.0: bios: version 86.07.39.00.bb
[ 138.697474] nouveau 0000:08:00.0: fb: 4096 MiB GDDR5
[ 139.981332] nouveau 0000:08:00.0: DRM: VRAM: 4096 MiB
[ 139.981334] nouveau 0000:08:00.0: DRM: GART: 536870912 MiB
[ 139.981337] nouveau 0000:08:00.0: DRM: BIT table 'A' not found
[ 139.981338] nouveau 0000:08:00.0: DRM: BIT table 'L' not found
[ 139.981340] nouveau 0000:08:00.0: DRM: TMDS table version 2.0
[ 139.981341] nouveau 0000:08:00.0: DRM: DCB version 4.1
[ 139.981343] nouveau 0000:08:00.0: DRM: DCB outp 00: 01000f42 04620030
[ 139.981345] nouveau 0000:08:00.0: DRM: DCB outp 01: 02011f62 04620010
[ 139.981347] nouveau 0000:08:00.0: DRM: DCB outp 02: 02822f76 04600020
[ 139.981348] nouveau 0000:08:00.0: DRM: DCB outp 03: 02022f72 04620020
[ 139.981350] nouveau 0000:08:00.0: DRM: DCB conn 00: 00001031
[ 139.981351] nouveau 0000:08:00.0: DRM: DCB conn 01: 00010161
[ 139.981352] nouveau 0000:08:00.0: DRM: DCB conn 02: 00020246
[ 140.003057] [drm] Supports vblank timestamp caching Rev 2 (21.10.2013).
[ 140.003058] [drm] Driver supports precise vblank timestamp query.
[ 140.066883] nouveau 0000:08:00.0: DRM: MM: using COPY for buffer copies
[ 140.681901] nouveau 0000:08:00.0: DRM: allocated 1280x1024 fb: 0x200000, bo 000000008e131786
[ 140.681908] checking generic (ef000000 500000) vs hw (0 0)
[ 140.682113] fbcon: nouveaufb (fb1) is primary device
[ 140.682115] fbcon: Remapping primary device, fb1, to tty 1-63
[ 140.852219] nouveau 0000:08:00.0: fb1: nouveaufb frame buffer device
[ 140.892129] [drm] Initialized nouveau 1.3.1 20120801 for 0000:08:00.0 on minor 1
[ 141.733094] IPv6: ADDRCONF(NETDEV_UP): enp2s0: link is not ready
[ 141.816589] IPv6: ADDRCONF(NETDEV_UP): enp2s0: link is not ready
[ 141.821559] IPv6: ADDRCONF(NETDEV_UP): enp3s0: link is not ready
[ 141.904273] IPv6: ADDRCONF(NETDEV_UP): enp3s0: link is not ready
[ 142.458283] amdgpu 0000:06:00.0: vgaarb: changed VGA decodes: olddecodes=io+mem,decodes=none:owns=none
[ 142.458287] nouveau 0000:08:00.0: vgaarb: changed VGA decodes: olddecodes=io+mem,decodes=none:owns=io+mem
[ 145.057138] e1000e: enp3s0 NIC Link is Up 1000 Mbps Full Duplex, Flow Control: Rx/Tx
[ 145.057511] IPv6: ADDRCONF(NETDEV_CHANGE): enp3s0: link becomes ready
[ 145.207360] nouveau 0000:08:00.0: gr: intr 00000040
[ 156.843495] systemd-journald[509]: File /var/log/journal/40d705ecb985487d87725bd5ed268b7c/user-1000.journal corrupted or uncleanly shut down, renaming and replacing.
[ 167.503117] rfkill: input handler disabled
[ 265.480820] [drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring sdma0 timeout, last signaled seq=26, last emitted seq=28
[ 265.480827] [drm] IP block:gmc_v8_0 is hung!
[ 265.480829] [drm] IP block:tonga_ih is hung!
[ 265.480831] [drm] IP block:gfx_v8_0 is hung!
[ 265.480832] [drm] IP block:sdma_v3_0 is hung!
[ 265.480833] [drm] IP block:uvd_v6_0 is hung!
[ 265.480835] [drm] IP block:vce_v3_0 is hung!
[ 265.480836] [drm] GPU recovery disabled.
[-- Attachment #3: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1ryiqqrxTr5mn+Y4VvNAn-LtQb-0cBTitKKoQb+4B1=Qg-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-05-25 10:23 ` Luís Mendes
[not found] ` <CAEzXK1ob33a28y_jwj_8ovr_ZDiowMAiUrnAQxS4vM5PK3NzzQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-05-25 10:23 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
[-- Attachment #1.1: Type: text/plain, Size: 3871 bytes --]
I've just tested Ubuntu 18.04 with kernel 4.17-rc6 using libdrm-2.4.92 and
mesa-18.1.0.
Now both sdma0 and sdma1 timeout as can be seen in the attached logs.
~agd5f -b drm-next-4.18 doesn't improve also.
I have also tried amdgpu-pro 18.20 both on Ubuntu 18.04 and 16.04, but no
improvements.
I have tried amdgpu-pro 18.10 and 17.50 and also no improvements.
./amdgpu-pro-install -opencl=legacy,pal --headless
On Thu, May 24, 2018 at 11:18 AM, Luís Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
wrote:
> Additional update...
>
> I was able to boot and enter X by installing an NVIDIA GTX 1050 Ti as the
> primary display card and using an AMD RX 550 as the secondary card on the
> Tyan S7025 with the same Ubuntu 18.04 and the same Linux kernel 4.17-rc6.
> However once I try to run an OpenCL kernel on RX 550 I get a sdma1 timeout
> and the GPU hangs, which likely what is happening when I boot with RX 550
> as the single GPU card on the system.
>
> This means it is not an issue introduced in 4.17-rc6, it just means that I
> didn't notice the effect of the system with the two GPUs vs system with
> single AMD GPU.
>
> The dmesg log follows attached.
>
> Luís
>
> On Thu, May 24, 2018 at 10:13 AM, Luís Mendes <luis.p.mendes@gmail.com>
> wrote:
>
>> Hi Michel,
>>
>> I also work as a researcher at a university and we are considering buying
>> AMD cards to do OpenCL computations for numerical modelling, but currently
>> I am unable to give a try at the AMD cards I have at home.
>> I couldn't find any working driver for them... also amdgpu-pro drivers
>> don't work, or at least I have been unable to make them work.
>>
>> Regards,
>> Luís
>>
>> On Thu, May 24, 2018 at 10:01 AM, Luís Mendes <luis.p.mendes@gmail.com>
>> wrote:
>>
>>> Hi Michel,
>>>
>>> So summarizing with Linux kernel 4.17-rc6 on Ubuntu 18.04 using AMD RX
>>> 460/RX 550 I am not able to enter X.
>>> The same system with AMD Radeon R7 240 not only enters X as also runs
>>> the OpenCL kernel that RX 460 / RX 550 are unable to run for all the
>>> kernels that I have tested.
>>> Could this also be a Mesa issue, regarding OpenCL on RX 460?
>>>
>>> Regards,
>>> Luís
>>>
>>> On Thu, May 24, 2018 at 9:55 AM, Luís Mendes <luis.p.mendes@gmail.com>
>>> wrote:
>>>
>>>> Hi Michel,
>>>>
>>>> I will have to check previous rc releases of 4.17 to see if it wasn't
>>>> already happening, before trying any possible git bisect.
>>>> As an update I can say that an AMD Radeon R7 240 works fine on the same
>>>> system with the same kernel and I am able to run the OpenCL kernels, that I
>>>> couldn't with RX 460/RX 550.
>>>>
>>>> Regards,
>>>> Luís
>>>>
>>>> On Thu, May 24, 2018 at 9:30 AM, Michel Dänzer <michel-otUistvHUpNNg+MwTxZMZA@public.gmane.orgt>
>>>> wrote:
>>>>
>>>>> On 2018-05-24 12:06 AM, Luís Mendes wrote:
>>>>> > I've tried Linux 4.17-rc6 with Ubuntu 18.04 on Tyan S7002 and I am
>>>>> not even
>>>>> > able see lightdm/gdm3 as system hangs when starting X.
>>>>> > Having SR-IOV enabled or disabled makes no difference.
>>>>> > Tested with AMD RX 460.
>>>>> > When X is supposed to start the system hangs and only a rectangular
>>>>> region
>>>>> > on the top left corner screen remains with console text messages
>>>>> from the
>>>>> > boot process while the remaining of the screen is just black. I am
>>>>> unable
>>>>> > to do anything with the keyboard, switching to console does not work,
>>>>> > ctrl-alt-del also doesn't work. I've to do a cold reset.
>>>>>
>>>>> Can you isolate which change introduced this new issue with git bisect?
>>>>>
>>>>>
>>>>> --
>>>>> Earthling Michel Dänzer |
>>>>> http://www.amd.com
>>>>> Libre software enthusiast | Mesa and X
>>>>> developer
>>>>>
>>>>
>>>>
>>>
>>
>
[-- Attachment #1.2: Type: text/html, Size: 6626 bytes --]
[-- Attachment #2: amdgpu_ubuntu18.04_kernel17-rc6_mesa18.1.0_libdrm2.4.92.txt --]
[-- Type: text/plain, Size: 76188 bytes --]
[ 0.000000] Linux version 4.17.0-rc6 (lpnm@lpnm-empty) (gcc version 7.3.0 (Ubuntu 7.3.0-16ubuntu3)) #1 SMP Mon May 21 00:03:25 WEST 2018
[ 0.000000] Command line: BOOT_IMAGE=/boot/vmlinuz-4.17.0-rc6 root=UUID=1fd09015-7f74-4838-bbbd-00bb887c940f ro quiet splash vt.handoff=1
[ 0.000000] KERNEL supported cpus:
[ 0.000000] Intel GenuineIntel
[ 0.000000] AMD AuthenticAMD
[ 0.000000] Centaur CentaurHauls
[ 0.000000] x86/fpu: x87 FPU will use FXSAVE
[ 0.000000] e820: BIOS-provided physical RAM map:
[ 0.000000] BIOS-e820: [mem 0x0000000000000000-0x000000000009d3ff] usable
[ 0.000000] BIOS-e820: [mem 0x000000000009d400-0x000000000009ffff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000000e0000-0x00000000000fffff] reserved
[ 0.000000] BIOS-e820: [mem 0x0000000000100000-0x00000000bf78ffff] usable
[ 0.000000] BIOS-e820: [mem 0x00000000bf790000-0x00000000bf79dfff] ACPI data
[ 0.000000] BIOS-e820: [mem 0x00000000bf79e000-0x00000000bf7cffff] ACPI NVS
[ 0.000000] BIOS-e820: [mem 0x00000000bf7d0000-0x00000000bf7dffff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000bf7ec000-0x00000000bfffffff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000e0000000-0x00000000efffffff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000fee00000-0x00000000fee00fff] reserved
[ 0.000000] BIOS-e820: [mem 0x00000000ffa00000-0x00000000ffffffff] reserved
[ 0.000000] BIOS-e820: [mem 0x0000000100000000-0x000000023fffffff] usable
[ 0.000000] NX (Execute Disable) protection: active
[ 0.000000] SMBIOS 2.6 present.
[ 0.000000] DMI: empty empty/S7002, BIOS 'V1.10B' 10/11/2011
[ 0.000000] e820: update [mem 0x00000000-0x00000fff] usable ==> reserved
[ 0.000000] e820: remove [mem 0x000a0000-0x000fffff] usable
[ 0.000000] e820: last_pfn = 0x240000 max_arch_pfn = 0x400000000
[ 0.000000] MTRR default type: uncachable
[ 0.000000] MTRR fixed ranges enabled:
[ 0.000000] 00000-9FFFF write-back
[ 0.000000] A0000-BFFFF uncachable
[ 0.000000] C0000-C7FFF write-protect
[ 0.000000] C8000-DFFFF uncachable
[ 0.000000] E0000-E3FFF write-protect
[ 0.000000] E4000-EFFFF write-through
[ 0.000000] F0000-FFFFF write-protect
[ 0.000000] MTRR variable ranges enabled:
[ 0.000000] 0 base 0000000000 mask FE00000000 write-back
[ 0.000000] 1 base 0200000000 mask FFC0000000 write-back
[ 0.000000] 2 base 00C0000000 mask FFC0000000 uncachable
[ 0.000000] 3 base 00BF800000 mask FFFF800000 uncachable
[ 0.000000] 4 disabled
[ 0.000000] 5 disabled
[ 0.000000] 6 disabled
[ 0.000000] 7 disabled
[ 0.000000] 8 disabled
[ 0.000000] 9 disabled
[ 0.000000] x86/PAT: Configuration [0-7]: WB WC UC- UC WB WP UC- WT
[ 0.000000] total RAM covered: 8184M
[ 0.000000] Found optimal setting for mtrr clean up
[ 0.000000] gran_size: 64K chunk_size: 16M num_reg: 5 lose cover RAM: 0G
[ 0.000000] e820: update [mem 0xbf800000-0xffffffff] usable ==> reserved
[ 0.000000] e820: last_pfn = 0xbf790 max_arch_pfn = 0x400000000
[ 0.000000] found SMP MP-table at [mem 0x000ff780-0x000ff78f] mapped at [ (ptrval)]
[ 0.000000] Scanning 1 areas for low memory corruption
[ 0.000000] Base memory trampoline at [ (ptrval)] 97000 size 24576
[ 0.000000] Using GB pages for direct mapping
[ 0.000000] BRK [0xa2f49000, 0xa2f49fff] PGTABLE
[ 0.000000] BRK [0xa2f4a000, 0xa2f4afff] PGTABLE
[ 0.000000] BRK [0xa2f4b000, 0xa2f4bfff] PGTABLE
[ 0.000000] BRK [0xa2f4c000, 0xa2f4cfff] PGTABLE
[ 0.000000] RAMDISK: [mem 0x31e3f000-0x34f16fff]
[ 0.000000] ACPI: Early table checksum verification disabled
[ 0.000000] ACPI: RSDP 0x00000000000FA9C0 000024 (v02 ACPIAM)
[ 0.000000] ACPI: XSDT 0x00000000BF790100 00005C (v01 101111 XSDT1628 20111011 MSFT 00000097)
[ 0.000000] ACPI: FACP 0x00000000BF790290 0000F4 (v03 101111 FACP1628 20111011 MSFT 00000097)
[ 0.000000] ACPI BIOS Warning (bug): 32/64X length mismatch in FADT/Gpe0Block: 128/64 (20180313/tbfadt-569)
[ 0.000000] ACPI: DSDT 0x00000000BF7904F0 0057F4 (v01 7002_ 7002_001 00000001 INTL 20051117)
[ 0.000000] ACPI: FACS 0x00000000BF79E000 000040
[ 0.000000] ACPI: FACS 0x00000000BF79E000 000040
[ 0.000000] ACPI: APIC 0x00000000BF790390 00011E (v01 101111 APIC1628 20111011 MSFT 00000097)
[ 0.000000] ACPI: MCFG 0x00000000BF7904B0 00003C (v01 101111 OEMMCFG 20111011 MSFT 00000097)
[ 0.000000] ACPI: OEMB 0x00000000BF79E040 00007A (v01 101111 OEMB1628 20111011 MSFT 00000097)
[ 0.000000] ACPI: HPET 0x00000000BF79A4F0 000038 (v01 101111 OEMHPET 20111011 MSFT 00000097)
[ 0.000000] ACPI: SRAT 0x00000000BF79A530 000250 (v01 101111 OEMSRAT 00000001 INTL 00000001)
[ 0.000000] ACPI: SSDT 0x00000000BF7A5780 000363 (v01 DpgPmm CpuPm 00000012 INTL 20051117)
[ 0.000000] ACPI: Local APIC address 0xfee00000
[ 0.000000] SRAT: PXM 0 -> APIC 0x00 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x02 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x04 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x10 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x12 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x14 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x01 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x03 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x05 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x11 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x13 -> Node 0
[ 0.000000] SRAT: PXM 0 -> APIC 0x15 -> Node 0
[ 0.000000] SRAT: PXM 1 -> APIC 0x20 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x22 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x24 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x30 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x32 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x34 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x21 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x23 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x25 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x31 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x33 -> Node 1
[ 0.000000] SRAT: PXM 1 -> APIC 0x35 -> Node 1
[ 0.000000] ACPI: SRAT: Node 0 PXM 0 [mem 0x00000000-0x0009ffff]
[ 0.000000] ACPI: SRAT: Node 0 PXM 0 [mem 0x00100000-0x7fffffff]
[ 0.000000] ACPI: SRAT: Node 1 PXM 1 [mem 0x80000000-0xbfffffff]
[ 0.000000] ACPI: SRAT: Node 1 PXM 1 [mem 0x100000000-0x23fffffff]
[ 0.000000] NUMA: Node 0 [mem 0x00000000-0x0009ffff] + [mem 0x00100000-0x7fffffff] -> [mem 0x00000000-0x7fffffff]
[ 0.000000] NUMA: Node 1 [mem 0x80000000-0xbfffffff] + [mem 0x100000000-0x23fffffff] -> [mem 0x80000000-0x23fffffff]
[ 0.000000] NODE_DATA(0) allocated [mem 0x7ffd5000-0x7fffffff]
[ 0.000000] NODE_DATA(1) allocated [mem 0x23ffd3000-0x23fffdfff]
[ 0.000000] tsc: Fast TSC calibration using PIT
[ 0.000000] Zone ranges:
[ 0.000000] DMA [mem 0x0000000000001000-0x0000000000ffffff]
[ 0.000000] DMA32 [mem 0x0000000001000000-0x00000000ffffffff]
[ 0.000000] Normal [mem 0x0000000100000000-0x000000023fffffff]
[ 0.000000] Device empty
[ 0.000000] Movable zone start for each node
[ 0.000000] Early memory node ranges
[ 0.000000] node 0: [mem 0x0000000000001000-0x000000000009cfff]
[ 0.000000] node 0: [mem 0x0000000000100000-0x000000007fffffff]
[ 0.000000] node 1: [mem 0x0000000080000000-0x00000000bf78ffff]
[ 0.000000] node 1: [mem 0x0000000100000000-0x000000023fffffff]
[ 0.000000] Initmem setup node 0 [mem 0x0000000000001000-0x000000007fffffff]
[ 0.000000] On node 0 totalpages: 524188
[ 0.000000] DMA zone: 64 pages used for memmap
[ 0.000000] DMA zone: 21 pages reserved
[ 0.000000] DMA zone: 3996 pages, LIFO batch:0
[ 0.000000] DMA32 zone: 8128 pages used for memmap
[ 0.000000] DMA32 zone: 520192 pages, LIFO batch:31
[ 0.000000] Initmem setup node 1 [mem 0x0000000080000000-0x000000023fffffff]
[ 0.000000] On node 1 totalpages: 1570704
[ 0.000000] DMA32 zone: 4063 pages used for memmap
[ 0.000000] DMA32 zone: 259984 pages, LIFO batch:31
[ 0.000000] Normal zone: 20480 pages used for memmap
[ 0.000000] Normal zone: 1310720 pages, LIFO batch:31
[ 0.000000] Reserved but unavailable: 100 pages
[ 0.000000] ACPI: PM-Timer IO Port: 0x808
[ 0.000000] ACPI: Local APIC address 0xfee00000
[ 0.000000] ACPI: LAPIC_NMI (acpi_id[0xff] high dfl lint[0x1])
[ 0.000000] IOAPIC[0]: apic_id 6, version 32, address 0xfec00000, GSI 0-23
[ 0.000000] IOAPIC[1]: apic_id 7, version 32, address 0xfec8a000, GSI 24-47
[ 0.000000] ACPI: INT_SRC_OVR (bus 0 bus_irq 0 global_irq 2 dfl dfl)
[ 0.000000] ACPI: INT_SRC_OVR (bus 0 bus_irq 9 global_irq 20 low level)
[ 0.000000] ACPI: IRQ0 used by override.
[ 0.000000] ACPI: IRQ9 used by override.
[ 0.000000] Using ACPI (MADT) for SMP configuration information
[ 0.000000] ACPI: HPET id: 0x8086a301 base: 0xfed00000
[ 0.000000] smpboot: Allowing 24 CPUs, 0 hotplug CPUs
[ 0.000000] PM: Registered nosave memory: [mem 0x00000000-0x00000fff]
[ 0.000000] PM: Registered nosave memory: [mem 0x0009d000-0x0009dfff]
[ 0.000000] PM: Registered nosave memory: [mem 0x0009e000-0x0009ffff]
[ 0.000000] PM: Registered nosave memory: [mem 0x000a0000-0x000dffff]
[ 0.000000] PM: Registered nosave memory: [mem 0x000e0000-0x000fffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf790000-0xbf79dfff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf79e000-0xbf7cffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf7d0000-0xbf7dffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf7e0000-0xbf7ebfff]
[ 0.000000] PM: Registered nosave memory: [mem 0xbf7ec000-0xbfffffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xc0000000-0xdfffffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xe0000000-0xefffffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xf0000000-0xfedfffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xfee00000-0xfee00fff]
[ 0.000000] PM: Registered nosave memory: [mem 0xfee01000-0xff9fffff]
[ 0.000000] PM: Registered nosave memory: [mem 0xffa00000-0xffffffff]
[ 0.000000] e820: [mem 0xc0000000-0xdfffffff] available for PCI devices
[ 0.000000] Booting paravirtualized kernel on bare hardware
[ 0.000000] clocksource: refined-jiffies: mask: 0xffffffff max_cycles: 0xffffffff, max_idle_ns: 7645519600211568 ns
[ 0.000000] random: get_random_bytes called from start_kernel+0x99/0x55a with crng_init=0
[ 0.000000] setup_percpu: NR_CPUS:8192 nr_cpumask_bits:24 nr_cpu_ids:24 nr_node_ids:2
[ 0.000000] percpu: Embedded 46 pages/cpu @ (ptrval) s151552 r8192 d28672 u262144
[ 0.000000] pcpu-alloc: s151552 r8192 d28672 u262144 alloc=1*2097152
[ 0.000000] pcpu-alloc: [0] 00 01 02 03 04 05 12 13 [0] 14 15 16 17 -- -- -- --
[ 0.000000] pcpu-alloc: [1] 06 07 08 09 10 11 18 19 [1] 20 21 22 23 -- -- -- --
[ 0.000000] Built 2 zonelists, mobility grouping on. Total pages: 2062136
[ 0.000000] Policy zone: Normal
[ 0.000000] Kernel command line: BOOT_IMAGE=/boot/vmlinuz-4.17.0-rc6 root=UUID=1fd09015-7f74-4838-bbbd-00bb887c940f ro quiet splash vt.handoff=1
[ 0.000000] Calgary: detecting Calgary via BIOS EBDA area
[ 0.000000] Calgary: Unable to locate Rio Grande table in EBDA - bailing!
[ 0.000000] Memory: 8099616K/8379568K available (12300K kernel code, 2520K rwdata, 4332K rodata, 2428K init, 2384K bss, 279952K reserved, 0K cma-reserved)
[ 0.000000] SLUB: HWalign=64, Order=0-3, MinObjects=0, CPUs=24, Nodes=2
[ 0.000000] Kernel/User page tables isolation: enabled
[ 0.000000] ftrace: allocating 40314 entries in 158 pages
[ 0.000000] Hierarchical RCU implementation.
[ 0.000000] RCU restricting CPUs from NR_CPUS=8192 to nr_cpu_ids=24.
[ 0.000000] Tasks RCU enabled.
[ 0.000000] RCU: Adjusting geometry for rcu_fanout_leaf=16, nr_cpu_ids=24
[ 0.000000] NR_IRQS: 524544, nr_irqs: 1024, preallocated irqs: 16
[ 0.000000] Console: colour dummy device 80x25
[ 0.000000] console [tty0] enabled
[ 0.000000] mempolicy: Enabling automatic NUMA balancing. Configure with numa_balancing= or the kernel.numa_balancing sysctl
[ 0.000000] ACPI: Core revision 20180313
[ 0.000000] clocksource: hpet: mask: 0xffffffff max_cycles: 0xffffffff, max_idle_ns: 133484882848 ns
[ 0.000000] hpet clockevent registered
[ 0.000000] APIC: Switch to symmetric I/O mode setup
[ 0.000000] Switched APIC routing to physical flat.
[ 0.000000] ..TIMER: vector=0x30 apic1=0 pin1=2 apic2=-1 pin2=-1
[ 0.020000] tsc: Fast TSC calibration using PIT
[ 0.024000] tsc: Detected 2933.701 MHz processor
[ 0.024000] clocksource: tsc-early: mask: 0xffffffffffffffff max_cycles: 0x2a499f26b1b, max_idle_ns: 440795325401 ns
[ 0.024000] Calibrating delay loop (skipped), value calculated using timer frequency.. 5867.40 BogoMIPS (lpj=11734804)
[ 0.024000] pid_max: default: 32768 minimum: 301
[ 0.024000] Security Framework initialized
[ 0.024000] Yama: becoming mindful.
[ 0.024000] AppArmor: AppArmor initialized
[ 0.024000] Dentry cache hash table entries: 1048576 (order: 11, 8388608 bytes)
[ 0.028245] Inode-cache hash table entries: 524288 (order: 10, 4194304 bytes)
[ 0.028299] Mount-cache hash table entries: 16384 (order: 5, 131072 bytes)
[ 0.028326] Mountpoint-cache hash table entries: 16384 (order: 5, 131072 bytes)
[ 0.028659] CPU: Physical Processor ID: 0
[ 0.028660] CPU: Processor Core ID: 0
[ 0.028670] mce: CPU supports 9 MCE banks
[ 0.028678] CPU0: Thermal monitoring enabled (TM1)
[ 0.028691] process: using mwait in idle threads
[ 0.028695] Last level iTLB entries: 4KB 512, 2MB 7, 4MB 7
[ 0.028696] Last level dTLB entries: 4KB 512, 2MB 32, 4MB 32, 1GB 0
[ 0.028698] Spectre V2 : Mitigation: Full generic retpoline
[ 0.028833] Freeing SMP alternatives memory: 36K
[ 0.036000] smpboot: CPU0: Intel(R) Xeon(R) CPU X5670 @ 2.93GHz (family: 0x6, model: 0x2c, stepping: 0x2)
[ 0.036000] Performance Events: PEBS fmt1+, Westmere events, 16-deep LBR, Intel PMU driver.
[ 0.036000] core: CPUID marked event: 'bus cycles' unavailable
[ 0.036000] ... version: 3
[ 0.036000] ... bit width: 48
[ 0.036000] ... generic registers: 4
[ 0.036000] ... value mask: 0000ffffffffffff
[ 0.036000] ... max period: 000000007fffffff
[ 0.036000] ... fixed-purpose events: 3
[ 0.036000] ... event mask: 000000070000000f
[ 0.036000] Hierarchical SRCU implementation.
[ 0.036000] smp: Bringing up secondary CPUs ...
[ 0.036000] x86: Booting SMP configuration:
[ 0.036000] .... node #0, CPUs: #1
[ 0.036914] NMI watchdog: Enabled. Permanently consumes one hw-PMU counter.
[ 0.036961] #2 #3 #4 #5
[ 0.048201] .... node #1, CPUs: #6 #7 #8 #9 #10 #11
[ 0.148144] .... node #0, CPUs: #12 #13 #14 #15 #16 #17
[ 0.164167] .... node #1, CPUs: #18 #19 #20 #21 #22 #23
[ 0.180051] smp: Brought up 2 nodes, 24 CPUs
[ 0.180051] smpboot: Max logical packages: 2
[ 0.180051] smpboot: Total of 24 processors activated (140812.21 BogoMIPS)
[ 0.185121] devtmpfs: initialized
[ 0.185121] x86/mm: Memory block size: 128MB
[ 0.185121] evm: security.selinux
[ 0.185121] evm: security.SMACK64
[ 0.185121] evm: security.SMACK64EXEC
[ 0.185121] evm: security.SMACK64TRANSMUTE
[ 0.185121] evm: security.SMACK64MMAP
[ 0.185121] evm: security.apparmor
[ 0.185121] evm: security.ima
[ 0.185121] evm: security.capability
[ 0.185121] PM: Registering ACPI NVS region [mem 0xbf79e000-0xbf7cffff] (204800 bytes)
[ 0.185121] clocksource: jiffies: mask: 0xffffffff max_cycles: 0xffffffff, max_idle_ns: 7645041785100000 ns
[ 0.185121] futex hash table entries: 8192 (order: 7, 524288 bytes)
[ 0.185121] pinctrl core: initialized pinctrl subsystem
[ 0.185121] RTC time: 10:00:30, date: 05/25/18
[ 0.189231] NET: Registered protocol family 16
[ 0.189332] audit: initializing netlink subsys (disabled)
[ 0.189339] audit: type=2000 audit(1527242429.188:1): state=initialized audit_enabled=0 res=1
[ 0.189339] cpuidle: using governor ladder
[ 0.189339] cpuidle: using governor menu
[ 0.189339] ACPI: bus type PCI registered
[ 0.189339] acpiphp: ACPI Hot Plug PCI Controller Driver version: 0.5
[ 0.189339] PCI: MMCONFIG for domain 0000 [bus 00-ff] at [mem 0xe0000000-0xefffffff] (base 0xe0000000)
[ 0.189339] PCI: MMCONFIG at [mem 0xe0000000-0xefffffff] reserved in E820
[ 0.189339] PCI: Using configuration type 1 for base access
[ 0.189764] HugeTLB registered 1.00 GiB page size, pre-allocated 0 pages
[ 0.189764] HugeTLB registered 2.00 MiB page size, pre-allocated 0 pages
[ 0.192158] ACPI: Added _OSI(Module Device)
[ 0.192159] ACPI: Added _OSI(Processor Device)
[ 0.192160] ACPI: Added _OSI(3.0 _SCP Extensions)
[ 0.192161] ACPI: Added _OSI(Processor Aggregator Device)
[ 0.192162] ACPI: Added _OSI(Linux-Dell-Video)
[ 0.196280] ACPI: 2 ACPI AML tables successfully acquired and loaded
[ 0.200293] ACPI: Dynamic OEM Table Load:
[ 0.200293] ACPI: SSDT 0xFFFF9984B8080000 00603C (v01 DpgPmm P001Ist 00000011 INTL 20051117)
[ 0.205255] ACPI: Dynamic OEM Table Load:
[ 0.205260] ACPI: SSDT 0xFFFF9984B80D3000 000C69 (v01 PmRef P001Cst 00003001 INTL 20051117)
[ 0.206149] ACPI: Dynamic OEM Table Load:
[ 0.206154] ACPI: SSDT 0xFFFF9984B80D1000 000A0A (v01 PmRef Cpu0Tst 00003000 INTL 20051117)
[ 0.206720] ACPI: Interpreter enabled
[ 0.206720] ACPI: (supports S0 S1 S3 S4 S5)
[ 0.206720] ACPI: Using IOAPIC for interrupt routing
[ 0.206720] PCI: Using host bridge windows from ACPI; if necessary, use "pci=nocrs" and report a bug
[ 0.206720] ACPI: Enabled 12 GPEs in block 00 to 3F
[ 0.218640] ACPI: PCI Root Bridge [PCI0] (domain 0000 [bus 00-ff])
[ 0.218646] acpi PNP0A08:00: _OSC: OS supports [ExtendedConfig ASPM ClockPM Segments MSI]
[ 0.218651] acpi PNP0A08:00: _OSC failed (AE_NOT_FOUND); disabling ASPM
[ 0.219019] PCI host bridge to bus 0000:00
[ 0.219022] pci_bus 0000:00: root bus resource [io 0x0000-0x0cf7 window]
[ 0.219023] pci_bus 0000:00: root bus resource [io 0x0d00-0xffff window]
[ 0.219025] pci_bus 0000:00: root bus resource [mem 0x000a0000-0x000bffff window]
[ 0.219026] pci_bus 0000:00: root bus resource [mem 0x000d0000-0x000dffff window]
[ 0.219028] pci_bus 0000:00: root bus resource [mem 0xc0000000-0xdfffffff window]
[ 0.219029] pci_bus 0000:00: root bus resource [mem 0xf0000000-0xfed8ffff window]
[ 0.219031] pci_bus 0000:00: root bus resource [bus 00-ff]
[ 0.219043] pci 0000:00:00.0: [8086:3403] type 00 class 0x060000
[ 0.219074] pci 0000:00:00.0: enabling Extended Tags
[ 0.219107] pci 0000:00:00.0: PME# supported from D0 D3hot D3cold
[ 0.219212] pci 0000:00:01.0: [8086:3408] type 01 class 0x060400
[ 0.219234] pci 0000:00:01.0: enabling Extended Tags
[ 0.219267] pci 0000:00:01.0: PME# supported from D0 D3hot D3cold
[ 0.219373] pci 0000:00:03.0: [8086:340a] type 01 class 0x060400
[ 0.219395] pci 0000:00:03.0: enabling Extended Tags
[ 0.219427] pci 0000:00:03.0: PME# supported from D0 D3hot D3cold
[ 0.219533] pci 0000:00:07.0: [8086:340e] type 01 class 0x060400
[ 0.219558] pci 0000:00:07.0: enabling Extended Tags
[ 0.219591] pci 0000:00:07.0: PME# supported from D0 D3hot D3cold
[ 0.219692] pci 0000:00:08.0: [8086:340f] type 01 class 0x060400
[ 0.219712] pci 0000:00:08.0: enabling Extended Tags
[ 0.219743] pci 0000:00:08.0: PME# supported from D0 D3hot D3cold
[ 0.219841] pci 0000:00:09.0: [8086:3410] type 01 class 0x060400
[ 0.219861] pci 0000:00:09.0: enabling Extended Tags
[ 0.219892] pci 0000:00:09.0: PME# supported from D0 D3hot D3cold
[ 0.219994] pci 0000:00:0a.0: [8086:3411] type 01 class 0x060400
[ 0.220019] pci 0000:00:0a.0: enabling Extended Tags
[ 0.220051] pci 0000:00:0a.0: PME# supported from D0 D3hot D3cold
[ 0.220153] pci 0000:00:13.0: [8086:342d] type 00 class 0x080020
[ 0.220164] pci 0000:00:13.0: reg 0x10: [mem 0xfec8a000-0xfec8afff]
[ 0.220206] pci 0000:00:13.0: PME# supported from D0 D3hot D3cold
[ 0.220293] pci 0000:00:14.0: [8086:342e] type 00 class 0x080000
[ 0.220420] pci 0000:00:14.1: [8086:3422] type 00 class 0x080000
[ 0.220554] pci 0000:00:14.2: [8086:3423] type 00 class 0x080000
[ 0.220679] pci 0000:00:14.3: [8086:3438] type 00 class 0x080000
[ 0.220792] pci 0000:00:16.0: [8086:3430] type 00 class 0x088000
[ 0.220806] pci 0000:00:16.0: reg 0x10: [mem 0xfbbd4000-0xfbbd7fff 64bit]
[ 0.220949] pci 0000:00:16.1: [8086:3431] type 00 class 0x088000
[ 0.220963] pci 0000:00:16.1: reg 0x10: [mem 0xfbbd8000-0xfbbdbfff 64bit]
[ 0.221095] pci 0000:00:16.2: [8086:3432] type 00 class 0x088000
[ 0.221109] pci 0000:00:16.2: reg 0x10: [mem 0xfbbdc000-0xfbbdffff 64bit]
[ 0.221242] pci 0000:00:16.3: [8086:3433] type 00 class 0x088000
[ 0.221256] pci 0000:00:16.3: reg 0x10: [mem 0xfbbe0000-0xfbbe3fff 64bit]
[ 0.221391] pci 0000:00:16.4: [8086:3429] type 00 class 0x088000
[ 0.221405] pci 0000:00:16.4: reg 0x10: [mem 0xfbbe4000-0xfbbe7fff 64bit]
[ 0.221537] pci 0000:00:16.5: [8086:342a] type 00 class 0x088000
[ 0.221551] pci 0000:00:16.5: reg 0x10: [mem 0xfbbe8000-0xfbbebfff 64bit]
[ 0.221683] pci 0000:00:16.6: [8086:342b] type 00 class 0x088000
[ 0.221696] pci 0000:00:16.6: reg 0x10: [mem 0xfbbec000-0xfbbeffff 64bit]
[ 0.221829] pci 0000:00:16.7: [8086:342c] type 00 class 0x088000
[ 0.221843] pci 0000:00:16.7: reg 0x10: [mem 0xfbbf0000-0xfbbf3fff 64bit]
[ 0.221976] pci 0000:00:1a.0: [8086:3a37] type 00 class 0x0c0300
[ 0.222016] pci 0000:00:1a.0: reg 0x20: [io 0x9400-0x941f]
[ 0.222140] pci 0000:00:1a.1: [8086:3a38] type 00 class 0x0c0300
[ 0.222180] pci 0000:00:1a.1: reg 0x20: [io 0x9480-0x949f]
[ 0.222302] pci 0000:00:1a.2: [8086:3a39] type 00 class 0x0c0300
[ 0.222342] pci 0000:00:1a.2: reg 0x20: [io 0x9800-0x981f]
[ 0.222474] pci 0000:00:1a.7: [8086:3a3c] type 00 class 0x0c0320
[ 0.222493] pci 0000:00:1a.7: reg 0x10: [mem 0xfbbf4000-0xfbbf43ff]
[ 0.222569] pci 0000:00:1a.7: PME# supported from D0 D3hot D3cold
[ 0.222667] pci 0000:00:1c.0: [8086:3a40] type 01 class 0x060400
[ 0.222731] pci 0000:00:1c.0: PME# supported from D0 D3hot D3cold
[ 0.222840] pci 0000:00:1c.4: [8086:3a48] type 01 class 0x060400
[ 0.222909] pci 0000:00:1c.4: PME# supported from D0 D3hot D3cold
[ 0.223017] pci 0000:00:1c.5: [8086:3a4a] type 01 class 0x060400
[ 0.223085] pci 0000:00:1c.5: PME# supported from D0 D3hot D3cold
[ 0.223191] pci 0000:00:1d.0: [8086:3a34] type 00 class 0x0c0300
[ 0.223231] pci 0000:00:1d.0: reg 0x20: [io 0x9880-0x989f]
[ 0.223352] pci 0000:00:1d.1: [8086:3a35] type 00 class 0x0c0300
[ 0.223392] pci 0000:00:1d.1: reg 0x20: [io 0x9c00-0x9c1f]
[ 0.223515] pci 0000:00:1d.2: [8086:3a36] type 00 class 0x0c0300
[ 0.223555] pci 0000:00:1d.2: reg 0x20: [io 0xa000-0xa01f]
[ 0.223682] pci 0000:00:1d.7: [8086:3a3a] type 00 class 0x0c0320
[ 0.223702] pci 0000:00:1d.7: reg 0x10: [mem 0xfbbf6000-0xfbbf63ff]
[ 0.223778] pci 0000:00:1d.7: PME# supported from D0 D3hot D3cold
[ 0.223880] pci 0000:00:1e.0: [8086:244e] type 01 class 0x060401
[ 0.224019] pci 0000:00:1f.0: [8086:3a16] type 00 class 0x060100
[ 0.224097] pci 0000:00:1f.0: quirk: [io 0x0800-0x087f] claimed by ICH6 ACPI/GPIO/TCO
[ 0.224101] pci 0000:00:1f.0: quirk: [io 0x0500-0x053f] claimed by ICH6 GPIO
[ 0.224104] pci 0000:00:1f.0: ICH7 LPC Generic IO decode 1 PIO at 0a00 (mask 00ff)
[ 0.224106] pci 0000:00:1f.0: ICH7 LPC Generic IO decode 2 PIO at 0ca0 (mask 000f)
[ 0.224225] pci 0000:00:1f.2: [8086:3a22] type 00 class 0x010601
[ 0.224241] pci 0000:00:1f.2: reg 0x10: [io 0xa880-0xa887]
[ 0.224248] pci 0000:00:1f.2: reg 0x14: [io 0xa800-0xa803]
[ 0.224254] pci 0000:00:1f.2: reg 0x18: [io 0xa480-0xa487]
[ 0.224261] pci 0000:00:1f.2: reg 0x1c: [io 0xa400-0xa403]
[ 0.224267] pci 0000:00:1f.2: reg 0x20: [io 0xa080-0xa09f]
[ 0.224274] pci 0000:00:1f.2: reg 0x24: [mem 0xfbbf8000-0xfbbf87ff]
[ 0.224311] pci 0000:00:1f.2: PME# supported from D3hot
[ 0.224405] pci 0000:00:1f.3: [8086:3a30] type 00 class 0x0c0500
[ 0.224422] pci 0000:00:1f.3: reg 0x10: [mem 0xfbbfa000-0xfbbfa0ff 64bit]
[ 0.224440] pci 0000:00:1f.3: reg 0x20: [io 0x0400-0x041f]
[ 0.224573] pci 0000:00:01.0: PCI bridge to [bus 0a]
[ 0.224612] pci 0000:00:03.0: PCI bridge to [bus 09]
[ 0.224658] pci 0000:08:00.0: [1002:67ef] type 00 class 0x030000
[ 0.224691] pci 0000:08:00.0: reg 0x10: [mem 0xd0000000-0xdfffffff 64bit pref]
[ 0.224702] pci 0000:08:00.0: reg 0x18: [mem 0xcfe00000-0xcfffffff 64bit pref]
[ 0.224709] pci 0000:08:00.0: reg 0x20: [io 0xe000-0xe0ff]
[ 0.224716] pci 0000:08:00.0: reg 0x24: [mem 0xfbe80000-0xfbebffff]
[ 0.224723] pci 0000:08:00.0: reg 0x30: [mem 0xfbe60000-0xfbe7ffff pref]
[ 0.224730] pci 0000:08:00.0: enabling Extended Tags
[ 0.224809] pci 0000:08:00.0: supports D1 D2
[ 0.224810] pci 0000:08:00.0: PME# supported from D1 D2 D3hot D3cold
[ 0.224918] pci 0000:08:00.1: [1002:aae0] type 00 class 0x040300
[ 0.224946] pci 0000:08:00.1: reg 0x10: [mem 0xfbefc000-0xfbefffff 64bit]
[ 0.224992] pci 0000:08:00.1: enabling Extended Tags
[ 0.225050] pci 0000:08:00.1: supports D1 D2
[ 0.225128] pci 0000:00:07.0: PCI bridge to [bus 08]
[ 0.225131] pci 0000:00:07.0: bridge window [io 0xe000-0xefff]
[ 0.225134] pci 0000:00:07.0: bridge window [mem 0xfbe00000-0xfbefffff]
[ 0.225137] pci 0000:00:07.0: bridge window [mem 0xcfe00000-0xdfffffff 64bit pref]
[ 0.225170] pci 0000:00:08.0: PCI bridge to [bus 07]
[ 0.225207] pci 0000:00:09.0: PCI bridge to [bus 06]
[ 0.225240] pci 0000:00:0a.0: PCI bridge to [bus 05]
[ 0.225293] pci 0000:00:1c.0: PCI bridge to [bus 04]
[ 0.225372] pci 0000:03:00.0: [8086:10d3] type 00 class 0x020000
[ 0.225412] pci 0000:03:00.0: reg 0x10: [mem 0xfbde0000-0xfbdfffff]
[ 0.225443] pci 0000:03:00.0: reg 0x18: [io 0xdc00-0xdc1f]
[ 0.225459] pci 0000:03:00.0: reg 0x1c: [mem 0xfbddc000-0xfbddffff]
[ 0.225605] pci 0000:03:00.0: PME# supported from D0 D3hot D3cold
[ 0.225715] pci 0000:00:1c.4: ASPM: current common clock configuration is broken, reconfiguring
[ 0.236027] pci 0000:00:1c.4: PCI bridge to [bus 03]
[ 0.236032] pci 0000:00:1c.4: bridge window [io 0xd000-0xdfff]
[ 0.236036] pci 0000:00:1c.4: bridge window [mem 0xfbd00000-0xfbdfffff]
[ 0.236124] pci 0000:02:00.0: [8086:10d3] type 00 class 0x020000
[ 0.236161] pci 0000:02:00.0: reg 0x10: [mem 0xfbce0000-0xfbcfffff]
[ 0.236192] pci 0000:02:00.0: reg 0x18: [io 0xcc00-0xcc1f]
[ 0.236208] pci 0000:02:00.0: reg 0x1c: [mem 0xfbcdc000-0xfbcdffff]
[ 0.236349] pci 0000:02:00.0: PME# supported from D0 D3hot D3cold
[ 0.236461] pci 0000:00:1c.5: ASPM: current common clock configuration is broken, reconfiguring
[ 0.248024] pci 0000:00:1c.5: PCI bridge to [bus 02]
[ 0.248029] pci 0000:00:1c.5: bridge window [io 0xc000-0xcfff]
[ 0.248033] pci 0000:00:1c.5: bridge window [mem 0xfbc00000-0xfbcfffff]
[ 0.248082] pci 0000:01:00.0: [1a03:2000] type 00 class 0x030000
[ 0.248101] pci 0000:01:00.0: reg 0x10: [mem 0xfb000000-0xfb7fffff]
[ 0.248110] pci 0000:01:00.0: reg 0x14: [mem 0xfafe0000-0xfaffffff]
[ 0.248118] pci 0000:01:00.0: reg 0x18: [io 0xbc00-0xbc7f]
[ 0.248176] pci 0000:01:00.0: supports D1 D2
[ 0.248177] pci 0000:01:00.0: PME# supported from D0 D1 D2 D3hot D3cold
[ 0.248252] pci 0000:00:1e.0: PCI bridge to [bus 01] (subtractive decode)
[ 0.248255] pci 0000:00:1e.0: bridge window [io 0xb000-0xbfff]
[ 0.248258] pci 0000:00:1e.0: bridge window [mem 0xfaf00000-0xfb7fffff]
[ 0.248262] pci 0000:00:1e.0: bridge window [io 0x0000-0x0cf7 window] (subtractive decode)
[ 0.248264] pci 0000:00:1e.0: bridge window [io 0x0d00-0xffff window] (subtractive decode)
[ 0.248265] pci 0000:00:1e.0: bridge window [mem 0x000a0000-0x000bffff window] (subtractive decode)
[ 0.248267] pci 0000:00:1e.0: bridge window [mem 0x000d0000-0x000dffff window] (subtractive decode)
[ 0.248268] pci 0000:00:1e.0: bridge window [mem 0xc0000000-0xdfffffff window] (subtractive decode)
[ 0.248269] pci 0000:00:1e.0: bridge window [mem 0xf0000000-0xfed8ffff window] (subtractive decode)
[ 0.249441] ACPI: PCI Interrupt Link [LNKA] (IRQs 3 4 6 7 *10 11 12 14 15)
[ 0.249513] ACPI: PCI Interrupt Link [LNKB] (IRQs *5)
[ 0.249581] ACPI: PCI Interrupt Link [LNKC] (IRQs 3 4 6 7 10 11 12 14 *15)
[ 0.249651] ACPI: PCI Interrupt Link [LNKD] (IRQs 3 4 6 7 10 *11 12 14 15)
[ 0.249721] ACPI: PCI Interrupt Link [LNKE] (IRQs 3 4 6 7 10 11 12 14 15) *0, disabled.
[ 0.249792] ACPI: PCI Interrupt Link [LNKF] (IRQs *3 4 6 7 10 11 12 14 15)
[ 0.249862] ACPI: PCI Interrupt Link [LNKG] (IRQs 3 4 6 7 10 11 12 14 15) *0, disabled.
[ 0.249934] ACPI: PCI Interrupt Link [LNKH] (IRQs 3 4 6 7 10 11 12 *14 15)
[ 0.250069] pci 0000:08:00.0: vgaarb: VGA device added: decodes=io+mem,owns=none,locks=none
[ 0.250069] pci 0000:01:00.0: vgaarb: setting as boot VGA device
[ 0.250069] pci 0000:01:00.0: vgaarb: VGA device added: decodes=io+mem,owns=io+mem,locks=none
[ 0.250069] pci 0000:01:00.0: vgaarb: bridge control possible
[ 0.250069] pci 0000:08:00.0: vgaarb: bridge control possible
[ 0.250069] vgaarb: loaded
[ 0.250069] SCSI subsystem initialized
[ 0.250069] libata version 3.00 loaded.
[ 0.250069] ACPI: bus type USB registered
[ 0.250069] usbcore: registered new interface driver usbfs
[ 0.250069] usbcore: registered new interface driver hub
[ 0.250069] usbcore: registered new device driver usb
[ 0.250069] pps_core: LinuxPPS API ver. 1 registered
[ 0.250069] pps_core: Software ver. 5.3.6 - Copyright 2005-2007 Rodolfo Giometti <giometti@linux.it>
[ 0.250069] PTP clock support registered
[ 0.250069] EDAC MC: Ver: 3.0.0
[ 0.252018] PCI: Using ACPI for IRQ routing
[ 0.256051] PCI: Discovered peer bus fe
[ 0.256052] PCI: root bus fe: using default resources
[ 0.256057] PCI: Probing PCI hardware (bus fe)
[ 0.256079] PCI host bridge to bus 0000:fe
[ 0.256081] pci_bus 0000:fe: root bus resource [io 0x0000-0xffff]
[ 0.256083] pci_bus 0000:fe: root bus resource [mem 0x00000000-0xffffffffff]
[ 0.256084] pci_bus 0000:fe: No busn resource found for root bus, will use [bus fe-ff]
[ 0.256087] pci_bus 0000:fe: busn_res: can not insert [bus fe-ff] under domain [bus 00-ff] (conflicts with (null) [bus 00-ff])
[ 0.256092] pci 0000:fe:00.0: [8086:2c70] type 00 class 0x060000
[ 0.256139] pci 0000:fe:00.1: [8086:2d81] type 00 class 0x060000
[ 0.256181] pci 0000:fe:02.0: [8086:2d90] type 00 class 0x060000
[ 0.256221] pci 0000:fe:02.1: [8086:2d91] type 00 class 0x060000
[ 0.256261] pci 0000:fe:02.2: [8086:2d92] type 00 class 0x060000
[ 0.256300] pci 0000:fe:02.3: [8086:2d93] type 00 class 0x060000
[ 0.256343] pci 0000:fe:02.4: [8086:2d94] type 00 class 0x060000
[ 0.256385] pci 0000:fe:02.5: [8086:2d95] type 00 class 0x060000
[ 0.256425] pci 0000:fe:03.0: [8086:2d98] type 00 class 0x060000
[ 0.256465] pci 0000:fe:03.1: [8086:2d99] type 00 class 0x060000
[ 0.256510] pci 0000:fe:03.2: [8086:2d9a] type 00 class 0x060000
[ 0.256553] pci 0000:fe:03.4: [8086:2d9c] type 00 class 0x060000
[ 0.256594] pci 0000:fe:04.0: [8086:2da0] type 00 class 0x060000
[ 0.256633] pci 0000:fe:04.1: [8086:2da1] type 00 class 0x060000
[ 0.256673] pci 0000:fe:04.2: [8086:2da2] type 00 class 0x060000
[ 0.256714] pci 0000:fe:04.3: [8086:2da3] type 00 class 0x060000
[ 0.256758] pci 0000:fe:05.0: [8086:2da8] type 00 class 0x060000
[ 0.256796] pci 0000:fe:05.1: [8086:2da9] type 00 class 0x060000
[ 0.256834] pci 0000:fe:05.2: [8086:2daa] type 00 class 0x060000
[ 0.256873] pci 0000:fe:05.3: [8086:2dab] type 00 class 0x060000
[ 0.256913] pci 0000:fe:06.0: [8086:2db0] type 00 class 0x060000
[ 0.256953] pci 0000:fe:06.1: [8086:2db1] type 00 class 0x060000
[ 0.256992] pci 0000:fe:06.2: [8086:2db2] type 00 class 0x060000
[ 0.257031] pci 0000:fe:06.3: [8086:2db3] type 00 class 0x060000
[ 0.257079] pci_bus 0000:fe: busn_res: [bus fe-ff] end is updated to fe
[ 0.257082] pci_bus 0000:fe: busn_res: can not insert [bus fe] under domain [bus 00-ff] (conflicts with (null) [bus 00-ff])
[ 0.257088] PCI: Discovered peer bus ff
[ 0.257089] PCI: root bus ff: using default resources
[ 0.257089] PCI: Probing PCI hardware (bus ff)
[ 0.257108] PCI host bridge to bus 0000:ff
[ 0.257110] pci_bus 0000:ff: root bus resource [io 0x0000-0xffff]
[ 0.257111] pci_bus 0000:ff: root bus resource [mem 0x00000000-0xffffffffff]
[ 0.257113] pci_bus 0000:ff: No busn resource found for root bus, will use [bus ff-ff]
[ 0.257115] pci_bus 0000:ff: busn_res: can not insert [bus ff] under domain [bus 00-ff] (conflicts with (null) [bus 00-ff])
[ 0.257119] pci 0000:ff:00.0: [8086:2c70] type 00 class 0x060000
[ 0.257155] pci 0000:ff:00.1: [8086:2d81] type 00 class 0x060000
[ 0.257195] pci 0000:ff:02.0: [8086:2d90] type 00 class 0x060000
[ 0.257230] pci 0000:ff:02.1: [8086:2d91] type 00 class 0x060000
[ 0.257265] pci 0000:ff:02.2: [8086:2d92] type 00 class 0x060000
[ 0.257301] pci 0000:ff:02.3: [8086:2d93] type 00 class 0x060000
[ 0.257336] pci 0000:ff:02.4: [8086:2d94] type 00 class 0x060000
[ 0.257375] pci 0000:ff:02.5: [8086:2d95] type 00 class 0x060000
[ 0.257414] pci 0000:ff:03.0: [8086:2d98] type 00 class 0x060000
[ 0.257450] pci 0000:ff:03.1: [8086:2d99] type 00 class 0x060000
[ 0.257485] pci 0000:ff:03.2: [8086:2d9a] type 00 class 0x060000
[ 0.257521] pci 0000:ff:03.4: [8086:2d9c] type 00 class 0x060000
[ 0.257559] pci 0000:ff:04.0: [8086:2da0] type 00 class 0x060000
[ 0.257594] pci 0000:ff:04.1: [8086:2da1] type 00 class 0x060000
[ 0.257630] pci 0000:ff:04.2: [8086:2da2] type 00 class 0x060000
[ 0.257666] pci 0000:ff:04.3: [8086:2da3] type 00 class 0x060000
[ 0.257703] pci 0000:ff:05.0: [8086:2da8] type 00 class 0x060000
[ 0.257741] pci 0000:ff:05.1: [8086:2da9] type 00 class 0x060000
[ 0.257776] pci 0000:ff:05.2: [8086:2daa] type 00 class 0x060000
[ 0.257813] pci 0000:ff:05.3: [8086:2dab] type 00 class 0x060000
[ 0.257852] pci 0000:ff:06.0: [8086:2db0] type 00 class 0x060000
[ 0.257895] pci 0000:ff:06.1: [8086:2db1] type 00 class 0x060000
[ 0.257935] pci 0000:ff:06.2: [8086:2db2] type 00 class 0x060000
[ 0.257974] pci 0000:ff:06.3: [8086:2db3] type 00 class 0x060000
[ 0.258020] pci_bus 0000:ff: busn_res: [bus ff] end is updated to ff
[ 0.258022] pci_bus 0000:ff: busn_res: can not insert [bus ff] under domain [bus 00-ff] (conflicts with (null) [bus 00-ff])
[ 0.258028] PCI: pci_cache_line_size set to 64 bytes
[ 0.258137] e820: reserve RAM buffer [mem 0x0009d400-0x0009ffff]
[ 0.258138] e820: reserve RAM buffer [mem 0xbf790000-0xbfffffff]
[ 0.258251] NetLabel: Initializing
[ 0.258252] NetLabel: domain hash size = 128
[ 0.258252] NetLabel: protocols = UNLABELED CIPSOv4 CALIPSO
[ 0.258268] NetLabel: unlabeled traffic allowed by default
[ 0.258282] hpet0: at MMIO 0xfed00000, IRQs 2, 8, 0, 0
[ 0.258282] hpet0: 4 comparators, 64-bit 14.318180 MHz counter
[ 0.260044] clocksource: Switched to clocksource tsc-early
[ 0.274454] VFS: Disk quotas dquot_6.6.0
[ 0.274486] VFS: Dquot-cache hash table entries: 512 (order 0, 4096 bytes)
[ 0.274624] AppArmor: AppArmor Filesystem Enabled
[ 0.274654] pnp: PnP ACPI init
[ 0.274779] system 00:00: [mem 0xfbf00000-0xfbffffff] has been reserved
[ 0.274781] system 00:00: [mem 0xfc000000-0xfcffffff] has been reserved
[ 0.274783] system 00:00: [mem 0xfd000000-0xfdffffff] has been reserved
[ 0.274785] system 00:00: [mem 0xfe000000-0xfebfffff] has been reserved
[ 0.274786] system 00:00: [mem 0xfec8a000-0xfec8afff] could not be reserved
[ 0.274788] system 00:00: [mem 0xfed10000-0xfed10fff] has been reserved
[ 0.274794] system 00:00: Plug and Play ACPI device, IDs PNP0c01 (active)
[ 0.274874] pnp 00:01: Plug and Play ACPI device, IDs PNP0b00 (active)
[ 0.275185] pnp 00:02: [dma 0 disabled]
[ 0.275241] pnp 00:02: Plug and Play ACPI device, IDs PNP0501 (active)
[ 0.275736] system 00:03: [io 0x0a00-0x0a0f] has been reserved
[ 0.275738] system 00:03: [io 0x0a10-0x0a1f] has been reserved
[ 0.275742] system 00:03: Plug and Play ACPI device, IDs PNP0c02 (active)
[ 0.275960] system 00:04: [io 0x04d0-0x04d1] has been reserved
[ 0.275962] system 00:04: [io 0x0800-0x087f] has been reserved
[ 0.275964] system 00:04: [io 0x0500-0x057f] could not be reserved
[ 0.275966] system 00:04: [mem 0xfed1c000-0xfed1ffff] has been reserved
[ 0.275968] system 00:04: [mem 0xfed20000-0xfed3ffff] has been reserved
[ 0.275970] system 00:04: [mem 0xfed40000-0xfed8ffff] has been reserved
[ 0.275974] system 00:04: Plug and Play ACPI device, IDs PNP0c02 (active)
[ 0.276170] system 00:05: [mem 0xfec00000-0xfec00fff] could not be reserved
[ 0.276172] system 00:05: [mem 0xfee00000-0xfee00fff] has been reserved
[ 0.276177] system 00:05: Plug and Play ACPI device, IDs PNP0c02 (active)
[ 0.276267] system 00:06: [mem 0xe0000000-0xefffffff] has been reserved
[ 0.276272] system 00:06: Plug and Play ACPI device, IDs PNP0c02 (active)
[ 0.276717] system 00:07: [mem 0x00000000-0x0009ffff] could not be reserved
[ 0.276719] system 00:07: [mem 0x000c0000-0x000cffff] could not be reserved
[ 0.276721] system 00:07: [mem 0x000e0000-0x000fffff] could not be reserved
[ 0.276722] system 00:07: [mem 0x00100000-0xbfffffff] could not be reserved
[ 0.276724] system 00:07: [mem 0xfed90000-0xffffffff] could not be reserved
[ 0.276729] system 00:07: Plug and Play ACPI device, IDs PNP0c01 (active)
[ 0.276892] pnp: PnP ACPI: found 8 devices
[ 0.282922] clocksource: acpi_pm: mask: 0xffffff max_cycles: 0xffffff, max_idle_ns: 2085701024 ns
[ 0.282962] pci 0000:00:1c.0: bridge window [io 0x1000-0x0fff] to [bus 04] add_size 1000
[ 0.282964] pci 0000:00:1c.0: bridge window [mem 0x00100000-0x000fffff 64bit pref] to [bus 04] add_size 200000 add_align 100000
[ 0.282966] pci 0000:00:1c.0: bridge window [mem 0x00100000-0x000fffff] to [bus 04] add_size 200000 add_align 100000
[ 0.282973] pci 0000:00:1c.4: bridge window [mem 0x00100000-0x000fffff 64bit pref] to [bus 03] add_size 200000 add_align 100000
[ 0.282980] pci 0000:00:1c.5: bridge window [mem 0x00100000-0x000fffff 64bit pref] to [bus 02] add_size 200000 add_align 100000
[ 0.282997] pci 0000:00:1c.0: BAR 14: assigned [mem 0xc0000000-0xc01fffff]
[ 0.283002] pci 0000:00:1c.0: BAR 15: assigned [mem 0xc0200000-0xc03fffff 64bit pref]
[ 0.283005] pci 0000:00:1c.4: BAR 15: assigned [mem 0xc0400000-0xc05fffff 64bit pref]
[ 0.283008] pci 0000:00:1c.5: BAR 15: assigned [mem 0xc0600000-0xc07fffff 64bit pref]
[ 0.283010] pci 0000:00:1c.0: BAR 13: assigned [io 0x1000-0x1fff]
[ 0.283013] pci 0000:00:01.0: PCI bridge to [bus 0a]
[ 0.283020] pci 0000:00:03.0: PCI bridge to [bus 09]
[ 0.283027] pci 0000:00:07.0: PCI bridge to [bus 08]
[ 0.283029] pci 0000:00:07.0: bridge window [io 0xe000-0xefff]
[ 0.283032] pci 0000:00:07.0: bridge window [mem 0xfbe00000-0xfbefffff]
[ 0.283034] pci 0000:00:07.0: bridge window [mem 0xcfe00000-0xdfffffff 64bit pref]
[ 0.283038] pci 0000:00:08.0: PCI bridge to [bus 07]
[ 0.283045] pci 0000:00:09.0: PCI bridge to [bus 06]
[ 0.283051] pci 0000:00:0a.0: PCI bridge to [bus 05]
[ 0.283059] pci 0000:00:1c.0: PCI bridge to [bus 04]
[ 0.283061] pci 0000:00:1c.0: bridge window [io 0x1000-0x1fff]
[ 0.283064] pci 0000:00:1c.0: bridge window [mem 0xc0000000-0xc01fffff]
[ 0.283067] pci 0000:00:1c.0: bridge window [mem 0xc0200000-0xc03fffff 64bit pref]
[ 0.283072] pci 0000:00:1c.4: PCI bridge to [bus 03]
[ 0.283074] pci 0000:00:1c.4: bridge window [io 0xd000-0xdfff]
[ 0.283077] pci 0000:00:1c.4: bridge window [mem 0xfbd00000-0xfbdfffff]
[ 0.283080] pci 0000:00:1c.4: bridge window [mem 0xc0400000-0xc05fffff 64bit pref]
[ 0.283084] pci 0000:00:1c.5: PCI bridge to [bus 02]
[ 0.283086] pci 0000:00:1c.5: bridge window [io 0xc000-0xcfff]
[ 0.283089] pci 0000:00:1c.5: bridge window [mem 0xfbc00000-0xfbcfffff]
[ 0.283092] pci 0000:00:1c.5: bridge window [mem 0xc0600000-0xc07fffff 64bit pref]
[ 0.283097] pci 0000:00:1e.0: PCI bridge to [bus 01]
[ 0.283099] pci 0000:00:1e.0: bridge window [io 0xb000-0xbfff]
[ 0.283102] pci 0000:00:1e.0: bridge window [mem 0xfaf00000-0xfb7fffff]
[ 0.283109] pci_bus 0000:00: resource 4 [io 0x0000-0x0cf7 window]
[ 0.283110] pci_bus 0000:00: resource 5 [io 0x0d00-0xffff window]
[ 0.283111] pci_bus 0000:00: resource 6 [mem 0x000a0000-0x000bffff window]
[ 0.283113] pci_bus 0000:00: resource 7 [mem 0x000d0000-0x000dffff window]
[ 0.283114] pci_bus 0000:00: resource 8 [mem 0xc0000000-0xdfffffff window]
[ 0.283115] pci_bus 0000:00: resource 9 [mem 0xf0000000-0xfed8ffff window]
[ 0.283117] pci_bus 0000:08: resource 0 [io 0xe000-0xefff]
[ 0.283118] pci_bus 0000:08: resource 1 [mem 0xfbe00000-0xfbefffff]
[ 0.283119] pci_bus 0000:08: resource 2 [mem 0xcfe00000-0xdfffffff 64bit pref]
[ 0.283121] pci_bus 0000:04: resource 0 [io 0x1000-0x1fff]
[ 0.283122] pci_bus 0000:04: resource 1 [mem 0xc0000000-0xc01fffff]
[ 0.283123] pci_bus 0000:04: resource 2 [mem 0xc0200000-0xc03fffff 64bit pref]
[ 0.283124] pci_bus 0000:03: resource 0 [io 0xd000-0xdfff]
[ 0.283126] pci_bus 0000:03: resource 1 [mem 0xfbd00000-0xfbdfffff]
[ 0.283127] pci_bus 0000:03: resource 2 [mem 0xc0400000-0xc05fffff 64bit pref]
[ 0.283128] pci_bus 0000:02: resource 0 [io 0xc000-0xcfff]
[ 0.283129] pci_bus 0000:02: resource 1 [mem 0xfbc00000-0xfbcfffff]
[ 0.283131] pci_bus 0000:02: resource 2 [mem 0xc0600000-0xc07fffff 64bit pref]
[ 0.283132] pci_bus 0000:01: resource 0 [io 0xb000-0xbfff]
[ 0.283133] pci_bus 0000:01: resource 1 [mem 0xfaf00000-0xfb7fffff]
[ 0.283134] pci_bus 0000:01: resource 4 [io 0x0000-0x0cf7 window]
[ 0.283136] pci_bus 0000:01: resource 5 [io 0x0d00-0xffff window]
[ 0.283137] pci_bus 0000:01: resource 6 [mem 0x000a0000-0x000bffff window]
[ 0.283138] pci_bus 0000:01: resource 7 [mem 0x000d0000-0x000dffff window]
[ 0.283139] pci_bus 0000:01: resource 8 [mem 0xc0000000-0xdfffffff window]
[ 0.283141] pci_bus 0000:01: resource 9 [mem 0xf0000000-0xfed8ffff window]
[ 0.283197] pci_bus 0000:fe: resource 4 [io 0x0000-0xffff]
[ 0.283198] pci_bus 0000:fe: resource 5 [mem 0x00000000-0xffffffffff]
[ 0.283202] pci_bus 0000:ff: resource 4 [io 0x0000-0xffff]
[ 0.283203] pci_bus 0000:ff: resource 5 [mem 0x00000000-0xffffffffff]
[ 0.283252] NET: Registered protocol family 2
[ 0.283522] tcp_listen_portaddr_hash hash table entries: 4096 (order: 4, 65536 bytes)
[ 0.283552] TCP established hash table entries: 65536 (order: 7, 524288 bytes)
[ 0.283691] TCP bind hash table entries: 65536 (order: 8, 1048576 bytes)
[ 0.283853] TCP: Hash tables configured (established 65536 bind 65536)
[ 0.283931] UDP hash table entries: 4096 (order: 5, 131072 bytes)
[ 0.283959] UDP-Lite hash table entries: 4096 (order: 5, 131072 bytes)
[ 0.284113] NET: Registered protocol family 1
[ 0.285830] pci 0000:08:00.1: Linked as a consumer to 0000:08:00.0
[ 0.285849] pci 0000:01:00.0: Video device with shadowed ROM at [mem 0x000c0000-0x000dffff]
[ 0.285909] PCI: CLS 256 bytes, default 64
[ 0.286001] Unpacking initramfs...
[ 1.003260] Freeing initrd memory: 50016K
[ 1.003314] PCI-DMA: Using software bounce buffering for IO (SWIOTLB)
[ 1.003317] software IO TLB [mem 0xbb790000-0xbf790000] (64MB) mapped at [ (ptrval)- (ptrval)]
[ 1.003965] Scanning for low memory corruption every 60 seconds
[ 1.004957] Initialise system trusted keyrings
[ 1.004969] Key type blacklist registered
[ 1.005022] workingset: timestamp_bits=36 max_order=21 bucket_order=0
[ 1.006398] zbud: loaded
[ 1.006968] squashfs: version 4.0 (2009/01/31) Phillip Lougher
[ 1.007173] fuse init (API version 7.26)
[ 1.007240] pstore: using deflate compression
[ 1.008273] Key type asymmetric registered
[ 1.008275] Asymmetric key parser 'x509' registered
[ 1.008306] Block layer SCSI generic (bsg) driver version 0.4 loaded (major 244)
[ 1.008358] io scheduler noop registered
[ 1.008359] io scheduler deadline registered
[ 1.008409] io scheduler cfq registered (default)
[ 1.008882] pcieport 0000:00:1c.0: enabling device (0104 -> 0107)
[ 1.009456] vesafb: mode is 1280x1024x32, linelength=5120, pages=0
[ 1.009457] vesafb: scrolling: redraw
[ 1.009459] vesafb: Truecolor: size=8:8:8:8, shift=24:16:8:0
[ 1.009471] vesafb: framebuffer at 0xfb000000, mapped to 0x (ptrval), using 5120k, total 5120k
[ 1.285167] Console: switching to colour frame buffer device 160x64
[ 1.561045] fb0: VESA VGA frame buffer device
[ 1.561059] intel_idle: MWAIT substates: 0x1120
[ 1.561060] intel_idle: v0.4.1 model 0x2C
[ 1.561920] intel_idle: lapic_timer_reliable_states 0xffffffff
[ 1.562011] input: Power Button as /devices/LNXSYSTM:00/LNXSYBUS:00/PNP0C0C:00/input/input0
[ 1.562033] ACPI: Power Button [PWRB]
[ 1.562072] input: Power Button as /devices/LNXSYSTM:00/LNXPWRBN:00/input/input1
[ 1.562079] ACPI: Power Button [PWRF]
[ 1.564836] Serial: 8250/16550 driver, 32 ports, IRQ sharing enabled
[ 1.585294] 00:02: ttyS0 at I/O 0x3f8 (irq = 4, base_baud = 115200) is a 16550A
[ 1.587599] Linux agpgart interface v0.103
[ 1.594832] loop: module loaded
[ 1.595401] libphy: Fixed MDIO Bus: probed
[ 1.595402] tun: Universal TUN/TAP device driver, 1.6
[ 1.595472] PPP generic driver version 2.4.2
[ 1.595544] ehci_hcd: USB 2.0 'Enhanced' Host Controller (EHCI) Driver
[ 1.595548] ehci-pci: EHCI PCI platform driver
[ 1.595704] ehci-pci 0000:00:1a.7: EHCI Host Controller
[ 1.595710] ehci-pci 0000:00:1a.7: new USB bus registered, assigned bus number 1
[ 1.595721] ehci-pci 0000:00:1a.7: debug port 1
[ 1.599631] ehci-pci 0000:00:1a.7: cache line size of 256 is not supported
[ 1.599645] ehci-pci 0000:00:1a.7: irq 18, io mem 0xfbbf4000
[ 1.612100] ehci-pci 0000:00:1a.7: USB 2.0 started, EHCI 1.00
[ 1.612171] usb usb1: New USB device found, idVendor=1d6b, idProduct=0002, bcdDevice= 4.17
[ 1.612174] usb usb1: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.612176] usb usb1: Product: EHCI Host Controller
[ 1.612179] usb usb1: Manufacturer: Linux 4.17.0-rc6 ehci_hcd
[ 1.612181] usb usb1: SerialNumber: 0000:00:1a.7
[ 1.612441] hub 1-0:1.0: USB hub found
[ 1.612452] hub 1-0:1.0: 6 ports detected
[ 1.612721] ehci-pci 0000:00:1d.7: EHCI Host Controller
[ 1.612726] ehci-pci 0000:00:1d.7: new USB bus registered, assigned bus number 2
[ 1.612735] ehci-pci 0000:00:1d.7: debug port 1
[ 1.616626] ehci-pci 0000:00:1d.7: cache line size of 256 is not supported
[ 1.616636] ehci-pci 0000:00:1d.7: irq 23, io mem 0xfbbf6000
[ 1.632100] ehci-pci 0000:00:1d.7: USB 2.0 started, EHCI 1.00
[ 1.632156] usb usb2: New USB device found, idVendor=1d6b, idProduct=0002, bcdDevice= 4.17
[ 1.632159] usb usb2: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.632161] usb usb2: Product: EHCI Host Controller
[ 1.632163] usb usb2: Manufacturer: Linux 4.17.0-rc6 ehci_hcd
[ 1.632166] usb usb2: SerialNumber: 0000:00:1d.7
[ 1.632406] hub 2-0:1.0: USB hub found
[ 1.632418] hub 2-0:1.0: 6 ports detected
[ 1.632562] ehci-platform: EHCI generic platform driver
[ 1.632569] ohci_hcd: USB 1.1 'Open' Host Controller (OHCI) Driver
[ 1.632572] ohci-pci: OHCI PCI platform driver
[ 1.632583] ohci-platform: OHCI generic platform driver
[ 1.632591] uhci_hcd: USB Universal Host Controller Interface driver
[ 1.632706] uhci_hcd 0000:00:1a.0: UHCI Host Controller
[ 1.632711] uhci_hcd 0000:00:1a.0: new USB bus registered, assigned bus number 3
[ 1.632717] uhci_hcd 0000:00:1a.0: detected 2 ports
[ 1.632740] uhci_hcd 0000:00:1a.0: irq 16, io base 0x00009400
[ 1.632787] usb usb3: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.632788] usb usb3: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.632790] usb usb3: Product: UHCI Host Controller
[ 1.632791] usb usb3: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.632792] usb usb3: SerialNumber: 0000:00:1a.0
[ 1.633051] hub 3-0:1.0: USB hub found
[ 1.633063] hub 3-0:1.0: 2 ports detected
[ 1.633285] uhci_hcd 0000:00:1a.1: UHCI Host Controller
[ 1.633289] uhci_hcd 0000:00:1a.1: new USB bus registered, assigned bus number 4
[ 1.633294] uhci_hcd 0000:00:1a.1: detected 2 ports
[ 1.633316] uhci_hcd 0000:00:1a.1: irq 21, io base 0x00009480
[ 1.633352] usb usb4: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.633354] usb usb4: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.633355] usb usb4: Product: UHCI Host Controller
[ 1.633356] usb usb4: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.633358] usb usb4: SerialNumber: 0000:00:1a.1
[ 1.633605] hub 4-0:1.0: USB hub found
[ 1.633616] hub 4-0:1.0: 2 ports detected
[ 1.633833] uhci_hcd 0000:00:1a.2: UHCI Host Controller
[ 1.633837] uhci_hcd 0000:00:1a.2: new USB bus registered, assigned bus number 5
[ 1.633842] uhci_hcd 0000:00:1a.2: detected 2 ports
[ 1.633870] uhci_hcd 0000:00:1a.2: irq 19, io base 0x00009800
[ 1.633907] usb usb5: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.633909] usb usb5: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.633910] usb usb5: Product: UHCI Host Controller
[ 1.633912] usb usb5: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.633913] usb usb5: SerialNumber: 0000:00:1a.2
[ 1.634153] hub 5-0:1.0: USB hub found
[ 1.634165] hub 5-0:1.0: 2 ports detected
[ 1.634375] uhci_hcd 0000:00:1d.0: UHCI Host Controller
[ 1.634384] uhci_hcd 0000:00:1d.0: new USB bus registered, assigned bus number 6
[ 1.634389] uhci_hcd 0000:00:1d.0: detected 2 ports
[ 1.634406] uhci_hcd 0000:00:1d.0: irq 23, io base 0x00009880
[ 1.634444] usb usb6: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.634446] usb usb6: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.634447] usb usb6: Product: UHCI Host Controller
[ 1.634448] usb usb6: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.634450] usb usb6: SerialNumber: 0000:00:1d.0
[ 1.634699] hub 6-0:1.0: USB hub found
[ 1.634710] hub 6-0:1.0: 2 ports detected
[ 1.634915] uhci_hcd 0000:00:1d.1: UHCI Host Controller
[ 1.634920] uhci_hcd 0000:00:1d.1: new USB bus registered, assigned bus number 7
[ 1.634926] uhci_hcd 0000:00:1d.1: detected 2 ports
[ 1.634942] uhci_hcd 0000:00:1d.1: irq 19, io base 0x00009c00
[ 1.634979] usb usb7: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.634980] usb usb7: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.634982] usb usb7: Product: UHCI Host Controller
[ 1.634983] usb usb7: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.634984] usb usb7: SerialNumber: 0000:00:1d.1
[ 1.635091] hub 7-0:1.0: USB hub found
[ 1.635096] hub 7-0:1.0: 2 ports detected
[ 1.635277] uhci_hcd 0000:00:1d.2: UHCI Host Controller
[ 1.635282] uhci_hcd 0000:00:1d.2: new USB bus registered, assigned bus number 8
[ 1.635287] uhci_hcd 0000:00:1d.2: detected 2 ports
[ 1.635304] uhci_hcd 0000:00:1d.2: irq 18, io base 0x0000a000
[ 1.635343] usb usb8: New USB device found, idVendor=1d6b, idProduct=0001, bcdDevice= 4.17
[ 1.635345] usb usb8: New USB device strings: Mfr=3, Product=2, SerialNumber=1
[ 1.635346] usb usb8: Product: UHCI Host Controller
[ 1.635347] usb usb8: Manufacturer: Linux 4.17.0-rc6 uhci_hcd
[ 1.635349] usb usb8: SerialNumber: 0000:00:1d.2
[ 1.635446] hub 8-0:1.0: USB hub found
[ 1.635451] hub 8-0:1.0: 2 ports detected
[ 1.635569] i8042: PNP: No PS/2 controller found.
[ 1.635569] i8042: Probing ports directly.
[ 1.638623] serio: i8042 KBD port at 0x60,0x64 irq 1
[ 1.638627] serio: i8042 AUX port at 0x60,0x64 irq 12
[ 1.638777] mousedev: PS/2 mouse device common for all mice
[ 1.639143] rtc_cmos 00:01: RTC can wake from S4
[ 1.639236] rtc rtc0: invalid alarm value: 2018-5-25 10:11:61
[ 1.639333] rtc_cmos 00:01: registered as rtc0
[ 1.639360] rtc_cmos 00:01: alarms up to one month, y3k, 114 bytes nvram, hpet irqs
[ 1.639377] i2c /dev entries driver
[ 1.639449] device-mapper: uevent: version 1.0.3
[ 1.639522] device-mapper: ioctl: 4.39.0-ioctl (2018-04-03) initialised: dm-devel@redhat.com
[ 1.641259] ledtrig-cpu: registered to indicate activity on CPUs
[ 1.642210] NET: Registered protocol family 10
[ 1.647203] Segment Routing with IPv6
[ 1.647233] NET: Registered protocol family 17
[ 1.647315] Key type dns_resolver registered
[ 1.650752] RAS: Correctable Errors collector initialized.
[ 1.650841] microcode: sig=0x206c2, pf=0x1, revision=0x14
[ 1.651999] microcode: Microcode Update Driver: v2.2.
[ 1.652015] sched_clock: Marking stable (1652001248, 0)->(1824410011, -172408763)
[ 1.669679] registered taskstats version 1
[ 1.669703] Loading compiled-in X.509 certificates
[ 1.672748] Loaded X.509 cert 'Build time autogenerated kernel key: 8a422d2124cd616d9582218b11710484582c209e'
[ 1.672782] zswap: loaded using pool lzo/zbud
[ 1.689614] Key type big_key registered
[ 1.689619] Key type trusted registered
[ 1.691547] Key type encrypted registered
[ 1.691551] AppArmor: AppArmor sha1 policy hashing enabled
[ 1.691555] ima: No TPM chip found, activating TPM-bypass! (rc=-19)
[ 1.691561] ima: Allocated hash algorithm: sha1
[ 1.691584] evm: HMAC attrs: 0x1
[ 1.692157] Magic number: 2:892:22
[ 1.692257] memory memory62: hash matches
[ 1.693283] rtc_cmos 00:01: setting system clock to 2018-05-25 10:00:31 UTC (1527242431)
[ 1.705035] Freeing unused kernel memory: 2428K
[ 1.728143] Write protecting the kernel read-only data: 20480k
[ 1.733508] Freeing unused kernel memory: 2008K
[ 1.738803] Freeing unused kernel memory: 1812K
[ 1.748615] x86/mm: Checked W+X mappings: passed, no W+X pages found.
[ 1.748615] x86/mm: Checking user space page tables
[ 1.758217] x86/mm: Checked W+X mappings: passed, no W+X pages found.
[ 1.854943] e1000e: Intel(R) PRO/1000 Network Driver - 3.2.6-k
[ 1.854944] e1000e: Copyright(c) 1999 - 2015 Intel Corporation.
[ 1.855186] e1000e 0000:03:00.0: Interrupt Throttling Rate (ints/sec) set to dynamic conservative mode
[ 1.865114] ahci 0000:00:1f.2: version 3.0
[ 1.865293] ahci 0000:00:1f.2: SSS flag set, parallel bus scan disabled
[ 1.865329] ahci 0000:00:1f.2: AHCI 0001.0200 32 slots 6 ports 3 Gbps 0x3f impl SATA mode
[ 1.865332] ahci 0000:00:1f.2: flags: 64bit ncq sntf stag pm led clo pio slum part ccc ems sxs
[ 1.910820] e1000e 0000:03:00.0 0000:03:00.0 (uninitialized): registered PHC clock
[ 1.924960] scsi host0: ahci
[ 1.925396] scsi host1: ahci
[ 1.925716] scsi host2: ahci
[ 1.926045] scsi host3: ahci
[ 1.926307] scsi host4: ahci
[ 1.926508] scsi host5: ahci
[ 1.926545] ata1: SATA max UDMA/133 abar m2048@0xfbbf8000 port 0xfbbf8100 irq 27
[ 1.926547] ata2: SATA max UDMA/133 abar m2048@0xfbbf8000 port 0xfbbf8180 irq 27
[ 1.926548] ata3: SATA max UDMA/133 abar m2048@0xfbbf8000 port 0xfbbf8200 irq 27
[ 1.926550] ata4: SATA max UDMA/133 abar m2048@0xfbbf8000 port 0xfbbf8280 irq 27
[ 1.926551] ata5: SATA max UDMA/133 abar m2048@0xfbbf8000 port 0xfbbf8300 irq 27
[ 1.926552] ata6: SATA max UDMA/133 abar m2048@0xfbbf8000 port 0xfbbf8380 irq 27
[ 1.966115] [drm] Using P2A bridge for configuration
[ 1.966118] [drm] AST 1100 detected
[ 1.966125] [drm] Analog VGA only
[ 1.966136] [drm] dram MCLK=204 Mhz type=0 bus_width=16 size=00800000
[ 1.966264] [TTM] Zone kernel: Available graphics memory: 4077958 kiB
[ 1.966264] [TTM] Zone dma32: Available graphics memory: 2097152 kiB
[ 1.966265] [TTM] Initializing pool allocator
[ 1.966268] [TTM] Initializing DMA pool allocator
[ 1.970071] e1000e 0000:03:00.0 eth0: (PCI Express:2.5GT/s:Width x1) 00:e0:81:d9:9b:a1
[ 1.970072] e1000e 0000:03:00.0 eth0: Intel(R) PRO/1000 Network Connection
[ 1.970157] e1000e 0000:03:00.0 eth0: MAC: 3, PHY: 8, PBA No: FFFFFF-0FF
[ 1.970309] e1000e 0000:02:00.0: Interrupt Throttling Rate (ints/sec) set to dynamic conservative mode
[ 1.972011] usb 2-1: new high-speed USB device number 2 using ehci-pci
[ 2.009211] [drm] amdgpu kernel modesetting enabled.
[ 2.012028] tsc: Refined TSC clocksource calibration: 2933.436 MHz
[ 2.012883] clocksource: tsc: mask: 0xffffffffffffffff max_cycles: 0x2a48a50322c, max_idle_ns: 440795287943 ns
[ 2.033203] clocksource: Switched to clocksource tsc
[ 2.033427] checking generic (fb000000 500000) vs hw (fb000000 800000)
[ 2.033428] fb: switching to astdrmfb from VESA VGA
[ 2.033451] Console: switching to colour dummy device 80x25
[ 2.033690] fbcon: astdrmfb (fb0) is primary device
[ 2.037124] AMD IOMMUv2 driver by Joerg Roedel <jroedel@suse.de>
[ 2.037125] AMD IOMMUv2 functionality not available on this system
[ 2.039746] e1000e 0000:02:00.0 0000:02:00.0 (uninitialized): registered PHC clock
[ 2.048872] CRAT table not found
[ 2.048875] Virtual CRAT table created for CPU
[ 2.048876] Parsing CRAT table with 2 nodes
[ 2.048877] Creating topology SYSFS entries
[ 2.048897] Topology: Add CPU node
[ 2.048897] Finished initializing topology
[ 2.048972] kfd kfd: Initialized module
[ 2.097554] e1000e 0000:02:00.0 eth1: (PCI Express:2.5GT/s:Width x1) 00:e0:81:d9:9b:a2
[ 2.097555] e1000e 0000:02:00.0 eth1: Intel(R) PRO/1000 Network Connection
[ 2.097639] e1000e 0000:02:00.0 eth1: MAC: 3, PHY: 8, PBA No: FFFFFF-0FF
[ 2.100990] e1000e 0000:03:00.0 enp3s0: renamed from eth0
[ 2.129538] usb 2-1: New USB device found, idVendor=18a5, idProduct=022e, bcdDevice= 1.00
[ 2.129540] usb 2-1: New USB device strings: Mfr=10, Product=11, SerialNumber=3
[ 2.129541] usb 2-1: Product: Portable USB 3.0 Drive
[ 2.129543] usb 2-1: Manufacturer: Verbatim
[ 2.129544] usb 2-1: SerialNumber: 20051C075244
[ 2.213428] Console: switching to colour frame buffer device 160x64
[ 2.238997] ata1: SATA link down (SStatus 0 SControl 300)
[ 2.394047] ast 0000:01:00.0: fb0: astdrmfb frame buffer device
[ 2.394142] amdgpu 0000:08:00.0: enabling device (0140 -> 0143)
[ 2.412117] [drm] Initialized ast 0.1.0 20120228 for 0000:01:00.0 on minor 0
[ 2.412302] e1000e 0000:02:00.0 enp2s0: renamed from eth1
[ 2.412450] [drm] initializing kernel modesetting (POLARIS11 0x1002:0x67EF 0x174B:0xE348 0xCF).
[ 2.412458] [drm] register mmio base: 0xFBE80000
[ 2.412459] [drm] register mmio size: 262144
[ 2.412465] [drm] probing gen 2 caps for device 8086:340e = 393042/0
[ 2.412467] [drm] probing mlw for device 8086:340e = 393042
[ 2.412468] [drm] add ip block number 0 <vi_common>
[ 2.412468] [drm] add ip block number 1 <gmc_v8_0>
[ 2.412469] [drm] add ip block number 2 <tonga_ih>
[ 2.412469] [drm] add ip block number 3 <powerplay>
[ 2.412470] [drm] add ip block number 4 <dm>
[ 2.412470] [drm] add ip block number 5 <gfx_v8_0>
[ 2.412471] [drm] add ip block number 6 <sdma_v3_0>
[ 2.412472] [drm] add ip block number 7 <uvd_v6_0>
[ 2.412472] [drm] add ip block number 8 <vce_v3_0>
[ 2.412475] kfd kfd: skipped device 1002:67ef, PCI rejects atomics
[ 2.412485] [drm] UVD is enabled in VM mode
[ 2.412485] [drm] UVD ENC is enabled in VM mode
[ 2.412487] [drm] VCE enabled in VM mode
[ 2.520074] usb 7-1: new low-speed USB device number 2 using uhci_hcd
[ 2.553082] ata2: SATA link up 1.5 Gbps (SStatus 113 SControl 300)
[ 2.555544] ata2.00: ATAPI: TSSTcorp CDDVDW SH-224FB, SB00, max UDMA/100
[ 2.556727] ata2.00: configured for UDMA/100
[ 2.558546] scsi 1:0:0:0: CD-ROM TSSTcorp CDDVDW SH-224FB SB00 PQ: 0 ANSI: 5
[ 2.635413] ATOM BIOS: 113-34801-U03
[ 2.635426] [drm] GPU posting now...
[ 2.748280] [drm] vm size is 64 GB, 2 levels, block size is 10-bit, fragment size is 9-bit
[ 2.748319] amdgpu 0000:08:00.0: VRAM: 2048M 0x000000F400000000 - 0x000000F47FFFFFFF (2048M used)
[ 2.748320] amdgpu 0000:08:00.0: GTT: 256M 0x0000000000000000 - 0x000000000FFFFFFF
[ 2.748324] [drm] Detected VRAM RAM=2048M, BAR=256M
[ 2.748324] [drm] RAM width 128bits GDDR5
[ 2.748340] [drm] amdgpu: 2048M of VRAM memory ready
[ 2.748341] [drm] amdgpu: 3072M of GTT memory ready.
[ 2.748349] [drm] GART: num cpu pages 65536, num gpu pages 65536
[ 2.748399] [drm] PCIE GART of 256M enabled (table at 0x000000F400040000).
[ 2.748519] [drm] Chained IB support enabled!
[ 2.751187] [drm] Found UVD firmware Version: 1.130 Family ID: 16
[ 2.752590] [drm] Found VCE firmware Version: 52.4 Binary ID: 3
[ 2.762411] sr 1:0:0:0: [sr0] scsi3-mmc drive: 47x/125x writer dvd-ram cd/rw xa/form2 cdda tray
[ 2.762413] cdrom: Uniform CD-ROM driver Revision: 3.20
[ 2.762613] sr 1:0:0:0: Attached scsi CD-ROM sr0
[ 2.762786] sr 1:0:0:0: Attached scsi generic sg0 type 5
[ 2.817341] amdgpu: [powerplay]
failed to send message 309 ret is 254
[ 2.817357] amdgpu: [powerplay]
failed to send pre message 14e ret is 254
[ 2.825498] [drm] DM_PPLIB: values for Engine clock
[ 2.825498] [drm] DM_PPLIB: 21400
[ 2.825499] [drm] DM_PPLIB: 48100
[ 2.825499] [drm] DM_PPLIB: 76000
[ 2.825500] [drm] DM_PPLIB: 102000
[ 2.825500] [drm] DM_PPLIB: 110200
[ 2.825500] [drm] DM_PPLIB: 113800
[ 2.825501] [drm] DM_PPLIB: 117200
[ 2.825501] [drm] DM_PPLIB: 121000
[ 2.825502] [drm] DM_PPLIB: Validation clocks:
[ 2.825502] [drm] DM_PPLIB: engine_max_clock: 121000
[ 2.825502] [drm] DM_PPLIB: memory_max_clock: 175000
[ 2.825503] [drm] DM_PPLIB: level : 0
[ 2.825504] [drm] DM_PPLIB: values for Memory clock
[ 2.825505] [drm] DM_PPLIB: 30000
[ 2.825505] [drm] DM_PPLIB: 175000
[ 2.825505] [drm] DM_PPLIB: Validation clocks:
[ 2.825506] [drm] DM_PPLIB: engine_max_clock: 121000
[ 2.825506] [drm] DM_PPLIB: memory_max_clock: 175000
[ 2.825506] [drm] DM_PPLIB: level : 0
[ 2.826404] [drm] Display Core initialized with v3.1.38!
[ 2.826891] [drm] Supports vblank timestamp caching Rev 2 (21.10.2013).
[ 2.826892] [drm] Driver supports precise vblank timestamp query.
[ 2.858678] [drm] UVD and UVD ENC initialized successfully.
[ 2.958611] [drm] VCE initialized successfully.
[ 3.003176] usb 7-1: New USB device found, idVendor=04d9, idProduct=1503, bcdDevice= 3.10
[ 3.003179] usb 7-1: New USB device strings: Mfr=1, Product=2, SerialNumber=0
[ 3.003182] usb 7-1: Product: USB Keyboard
[ 3.003184] usb 7-1: Manufacturer:
[ 3.020369] hidraw: raw HID events driver (C) Jiri Kosina
[ 3.075410] ata3: SATA link down (SStatus 0 SControl 300)
[ 3.146386] usbcore: registered new interface driver usbhid
[ 3.146386] usbhid: USB HID core driver
[ 3.157780] input: USB Keyboard as /devices/pci0000:00/0000:00:1d.1/usb7/7-1/7-1:1.0/0003:04D9:1503.0001/input/input5
[ 3.216440] hid-generic 0003:04D9:1503.0001: input,hidraw0: USB HID v1.10 Keyboard [ USB Keyboard] on usb-0000:00:1d.1-1/input0
[ 3.216588] input: USB Keyboard as /devices/pci0000:00/0000:00:1d.1/usb7/7-1/7-1:1.1/0003:04D9:1503.0002/input/input6
[ 3.276537] hid-generic 0003:04D9:1503.0002: input,hidraw1: USB HID v1.10 Device [ USB Keyboard] on usb-0000:00:1d.1-1/input1
[ 3.391817] ata4: SATA link down (SStatus 0 SControl 300)
[ 3.400095] usb 7-2: new low-speed USB device number 3 using uhci_hcd
[ 3.492287] [drm] Cannot find any crtc or sizes
[ 3.494696] [drm] Initialized amdgpu 3.25.0 20150101 for 0000:08:00.0 on minor 1
[ 3.594176] usb 7-2: New USB device found, idVendor=093a, idProduct=2510, bcdDevice= 1.00
[ 3.594179] usb 7-2: New USB device strings: Mfr=1, Product=2, SerialNumber=0
[ 3.594182] usb 7-2: Product: USB Optical Mouse
[ 3.594184] usb 7-2: Manufacturer: PixArt
[ 3.609393] input: PixArt USB Optical Mouse as /devices/pci0000:00/0000:00:1d.1/usb7/7-2/7-2:1.0/0003:093A:2510.0003/input/input7
[ 3.609876] hid-generic 0003:093A:2510.0003: input,hidraw2: USB HID v1.11 Mouse [PixArt USB Optical Mouse] on usb-0000:00:1d.1-2/input0
[ 3.707766] ata5: SATA link up 3.0 Gbps (SStatus 123 SControl 300)
[ 3.713779] ata5.00: ATA-8: SAMSUNG HD103SJ, 1AJ100E4, max UDMA/133
[ 3.713782] ata5.00: 1953525168 sectors, multi 0: LBA48 NCQ (depth 31/32), AA
[ 3.719945] ata5.00: configured for UDMA/133
[ 3.720385] scsi 4:0:0:0: Direct-Access ATA SAMSUNG HD103SJ 00E4 PQ: 0 ANSI: 5
[ 3.720972] sd 4:0:0:0: Attached scsi generic sg1 type 0
[ 3.721249] sd 4:0:0:0: [sda] 1953525168 512-byte logical blocks: (1.00 TB/932 GiB)
[ 3.721279] sd 4:0:0:0: [sda] Write Protect is off
[ 3.721282] sd 4:0:0:0: [sda] Mode Sense: 00 3a 00 00
[ 3.721329] sd 4:0:0:0: [sda] Write cache: enabled, read cache: enabled, doesn't support DPO or FUA
[ 3.776097] usb 2-5: new high-speed USB device number 5 using ehci-pci
[ 3.781216] sda: sda1 sda2 < sda5 sda6 sda7 sda8 > sda3 sda4
[ 3.782907] sd 4:0:0:0: [sda] Attached SCSI disk
[ 3.949265] usb 2-5: New USB device found, idVendor=046b, idProduct=ff01, bcdDevice= 1.00
[ 3.949267] usb 2-5: New USB device strings: Mfr=1, Product=2, SerialNumber=3
[ 3.949268] usb 2-5: Product: Generic Hub
[ 3.949269] usb 2-5: Manufacturer: American Megatrends Inc.
[ 3.949270] usb 2-5: SerialNumber: serial
[ 3.950232] hub 2-5:1.0: USB hub found
[ 3.950473] hub 2-5:1.0: 3 ports detected
[ 4.035712] ata6: SATA link down (SStatus 0 SControl 300)
[ 4.236081] usb 2-5.1: new low-speed USB device number 6 using ehci-pci
[ 4.250438] usb-storage 2-1:1.0: USB Mass Storage device detected
[ 4.250888] scsi host6: usb-storage 2-1:1.0
[ 4.251009] usbcore: registered new interface driver usb-storage
[ 4.260217] usbcore: registered new interface driver uas
[ 4.318068] random: fast init done
[ 4.358259] usb 2-5.1: New USB device found, idVendor=046b, idProduct=ff10, bcdDevice= 1.00
[ 4.358262] usb 2-5.1: New USB device strings: Mfr=1, Product=2, SerialNumber=3
[ 4.358265] usb 2-5.1: Product: Virtual Keyboard and Mouse
[ 4.358267] usb 2-5.1: Manufacturer: American Megatrends Inc.
[ 4.358269] usb 2-5.1: SerialNumber: serial
[ 4.360745] input: American Megatrends Inc. Virtual Keyboard and Mouse as /devices/pci0000:00/0000:00:1d.7/usb2/2-5/2-5.1/2-5.1:1.0/0003:046B:FF10.0004/input/input8
[ 4.360877] hid-generic 0003:046B:FF10.0004: input,hidraw3: USB HID v1.10 Keyboard [American Megatrends Inc. Virtual Keyboard and Mouse] on usb-0000:00:1d.7-5.1/input0
[ 4.362364] input: American Megatrends Inc. Virtual Keyboard and Mouse as /devices/pci0000:00/0000:00:1d.7/usb2/2-5/2-5.1/2-5.1:1.1/0003:046B:FF10.0005/input/input9
[ 4.362578] hid-generic 0003:046B:FF10.0005: input,hidraw4: USB HID v1.10 Mouse [American Megatrends Inc. Virtual Keyboard and Mouse] on usb-0000:00:1d.7-5.1/input1
[ 5.277479] scsi 6:0:0:0: Direct-Access Hitachi HTS543216L9A300 0100 PQ: 0 ANSI: 2 CCS
[ 5.278099] sd 6:0:0:0: Attached scsi generic sg2 type 0
[ 5.279329] sd 6:0:0:0: [sdb] 312581808 512-byte logical blocks: (160 GB/149 GiB)
[ 5.280680] sd 6:0:0:0: [sdb] Write Protect is off
[ 5.280682] sd 6:0:0:0: [sdb] Mode Sense: 28 00 00 00
[ 5.281872] sd 6:0:0:0: [sdb] No Caching mode page found
[ 5.281935] sd 6:0:0:0: [sdb] Assuming drive cache: write through
[ 5.336185] sdb: sdb1 sdb2 < sdb5 sdb6 >
[ 5.340944] sd 6:0:0:0: [sdb] Attached SCSI disk
[ 6.279887] EXT4-fs (sdb1): mounted filesystem with ordered data mode. Opts: (null)
[ 6.962597] random: crng init done
[ 8.277834] systemd[1]: systemd 237 running in system mode. (+PAM +AUDIT +SELINUX +IMA +APPARMOR +SMACK +SYSVINIT +UTMP +LIBCRYPTSETUP +GCRYPT +GNUTLS +ACL +XZ +LZ4 +SECCOMP +BLKID +ELFUTILS +KMOD -IDN2 +IDN -PCRE2 default-hierarchy=hybrid)
[ 8.297515] systemd[1]: Detected architecture x86-64.
[ 8.535638] systemd[1]: Set hostname to <lpnm-empty>.
[ 11.339217] systemd[1]: Started Forward Password Requests to Wall Directory Watch.
[ 11.339391] systemd[1]: Set up automount Arbitrary Executable File Formats File System Automount Point.
[ 11.339548] systemd[1]: Created slice User and Session Slice.
[ 11.339559] systemd[1]: Reached target User and Group Name Lookups.
[ 11.339566] systemd[1]: Reached target Remote File Systems.
[ 11.339688] systemd[1]: Created slice System Slice.
[ 11.339749] systemd[1]: Listening on /dev/initctl Compatibility Named Pipe.
[ 12.556841] EXT4-fs (sdb1): re-mounted. Opts: errors=remount-ro
[ 21.769467] systemd-journald[468]: Received request to flush runtime journal from PID 1
[ 21.914512] lp: driver loaded but no devices found
[ 22.346075] ipmi message handler version 39.2
[ 22.384870] ipmi device interface
[ 22.456234] ppdev: user-space parallel port driver
[ 22.655335] EDAC MC1: Giving out device to module i7core_edac.c controller i7 core #1: DEV 0000:fe:03.0 (INTERRUPT)
[ 22.655492] EDAC PCI0: Giving out device to module i7core_edac controller EDAC PCI controller: DEV 0000:fe:03.0 (POLLED)
[ 22.655714] EDAC MC0: Giving out device to module i7core_edac.c controller i7 core #0: DEV 0000:ff:03.0 (INTERRUPT)
[ 22.655744] EDAC PCI1: Giving out device to module i7core_edac controller EDAC PCI controller: DEV 0000:ff:03.0 (POLLED)
[ 22.655764] EDAC i7core: Driver loaded, 2 memory controller(s) found.
[ 22.675511] i5500_temp 0000:00:14.3: Sensor seems to be disabled
[ 22.851003] IPMI System Interface driver.
[ 22.851017] ipmi_si dmi-ipmi-si.0: ipmi_platform: probing via SMBIOS
[ 22.851018] ipmi_si: SMBIOS: io 0xca8 regsize 1 spacing 4 irq 0
[ 22.851022] ipmi_si: Adding SMBIOS-specified kcs state machine
[ 22.851048] ipmi_si IPI0001:00: ipmi_platform: probing via ACPI
[ 22.851077] ipmi_si IPI0001:00: [io 0x0ca8] regsize 1 spacing 4 irq 0
[ 22.851078] ipmi_si dmi-ipmi-si.0: Removing SMBIOS-specified kcs state machine in favor of ACPI
[ 22.868850] dca service started, version 1.12.1
[ 22.884054] ipmi_si: Adding ACPI-specified kcs state machine
[ 22.884106] ipmi_si: Trying ACPI-specified kcs state machine at i/o address 0xca8, slave address 0x20, irq 0
[ 22.912412] ioatdma: Intel(R) QuickData Technology Driver 4.00
[ 23.216423] ipmi_si IPI0001:00: Found new BMC (man_id: 0x0019fd, prod_id: 0x1b5a, dev_id: 0x20)
[ 23.257100] ipmi_si IPI0001:00: IPMI kcs interface initialized
[ 24.363515] gpio_ich: GPIO from 451 to 511 on gpio_ich
[ 24.371631] IPMI SSIF Interface driver
[ 24.386258] shpchp: Standard Hot Plug PCI Controller Driver version: 0.4
[ 24.709375] cryptd: max_cpu_qlen set to 1000
[ 26.063753] SSE version of gcm_enc/dec engaged.
[ 26.722497] kvm: VM_EXIT_LOAD_IA32_PERF_GLOBAL_CTRL does not work properly. Using workaround
[ 27.084507] snd_hda_intel 0000:08:00.1: Handle vga_switcheroo audio client
[ 27.084508] snd_hda_intel 0000:08:00.1: Force to non-snoop mode
[ 27.377806] input: HDA ATI HDMI HDMI/DP,pcm=3 as /devices/pci0000:00/0000:00:07.0/0000:08:00.1/sound/card0/input10
[ 27.377856] input: HDA ATI HDMI HDMI/DP,pcm=7 as /devices/pci0000:00/0000:00:07.0/0000:08:00.1/sound/card0/input11
[ 27.377900] input: HDA ATI HDMI HDMI/DP,pcm=8 as /devices/pci0000:00/0000:00:07.0/0000:08:00.1/sound/card0/input12
[ 27.377944] input: HDA ATI HDMI HDMI/DP,pcm=9 as /devices/pci0000:00/0000:00:07.0/0000:08:00.1/sound/card0/input13
[ 27.377993] input: HDA ATI HDMI HDMI/DP,pcm=10 as /devices/pci0000:00/0000:00:07.0/0000:08:00.1/sound/card0/input14
[ 30.512265] Adding 7815584k swap on /dev/sda8. Priority:-2 extents:1 across:7815584k FS
[ 30.894641] Adding 2440188k swap on /dev/sdb5. Priority:-3 extents:1 across:2440188k FS
[ 32.237921] EXT4-fs (sdb6): mounted filesystem with ordered data mode. Opts: (null)
[ 34.038642] audit: type=1400 audit(1527242463.840:2): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/snap/core/4650/usr/lib/snapd/snap-confine" pid=975 comm="apparmor_parser"
[ 34.038647] audit: type=1400 audit(1527242463.840:3): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/snap/core/4650/usr/lib/snapd/snap-confine//mount-namespace-capture-helper" pid=975 comm="apparmor_parser"
[ 34.069053] audit: type=1400 audit(1527242463.872:4): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/lib/lightdm/lightdm-guest-session" pid=973 comm="apparmor_parser"
[ 34.069057] audit: type=1400 audit(1527242463.872:5): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/lib/lightdm/lightdm-guest-session//chromium" pid=973 comm="apparmor_parser"
[ 34.070414] audit: type=1400 audit(1527242463.872:6): apparmor="STATUS" operation="profile_load" profile="unconfined" name="libreoffice-senddoc" pid=980 comm="apparmor_parser"
[ 34.070417] audit: type=1400 audit(1527242463.872:7): apparmor="STATUS" operation="profile_load" profile="unconfined" name="libreoffice-senddoc//sanitized_helper" pid=980 comm="apparmor_parser"
[ 34.072608] audit: type=1400 audit(1527242463.876:8): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/lib/snapd/snap-confine" pid=983 comm="apparmor_parser"
[ 34.072612] audit: type=1400 audit(1527242463.876:9): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/lib/snapd/snap-confine//mount-namespace-capture-helper" pid=983 comm="apparmor_parser"
[ 34.074231] audit: type=1400 audit(1527242463.876:10): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/usr/sbin/tcpdump" pid=988 comm="apparmor_parser"
[ 34.080474] audit: type=1400 audit(1527242463.884:11): apparmor="STATUS" operation="profile_load" profile="unconfined" name="/sbin/dhclient" pid=974 comm="apparmor_parser"
[ 42.026588] IPv6: ADDRCONF(NETDEV_UP): enp2s0: link is not ready
[ 42.104677] IPv6: ADDRCONF(NETDEV_UP): enp2s0: link is not ready
[ 42.110468] IPv6: ADDRCONF(NETDEV_UP): enp3s0: link is not ready
[ 42.188636] IPv6: ADDRCONF(NETDEV_UP): enp3s0: link is not ready
[ 43.830510] amdgpu 0000:08:00.0: vgaarb: changed VGA decodes: olddecodes=io+mem,decodes=none:owns=none
[ 45.221105] e1000e: enp3s0 NIC Link is Up 1000 Mbps Full Duplex, Flow Control: Rx/Tx
[ 45.221463] IPv6: ADDRCONF(NETDEV_CHANGE): enp3s0: link becomes ready
[ 83.992935] rfkill: input handler disabled
[ 90.484495] ISO 9660 Extensions: Microsoft Joliet Level 3
[ 90.516019] ISO 9660 Extensions: RRIP_1991A
[ 132.554661] [drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring sdma0 timeout, last signaled seq=26, last emitted seq=29
[ 132.554750] [drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring sdma1 timeout, last signaled seq=22, last emitted seq=24
[ 132.554753] [drm] IP block:gmc_v8_0 is hung!
[ 132.554756] [drm] IP block:gmc_v8_0 is hung!
[ 132.554758] [drm] IP block:tonga_ih is hung!
[ 132.554759] [drm] IP block:tonga_ih is hung!
[ 132.554761] [drm] IP block:gfx_v8_0 is hung!
[ 132.554762] [drm] IP block:gfx_v8_0 is hung!
[ 132.554763] [drm] IP block:sdma_v3_0 is hung!
[ 132.554764] [drm] IP block:sdma_v3_0 is hung!
[ 132.554766] [drm] IP block:uvd_v6_0 is hung!
[ 132.554767] [drm] IP block:uvd_v6_0 is hung!
[ 132.554769] [drm] IP block:vce_v3_0 is hung!
[ 132.554770] [drm] IP block:vce_v3_0 is hung!
[ 132.554771] [drm] GPU recovery disabled.
[ 132.554772] [drm] GPU recovery disabled.
[-- Attachment #3: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1ob33a28y_jwj_8ovr_ZDiowMAiUrnAQxS4vM5PK3NzzQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-06-26 9:03 ` Luís Mendes
[not found] ` <CAEzXK1oTc9p5hS97qNQHaW3Z82FXsDprSpfG4qVDhwT6VAaOhQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
0 siblings, 1 reply; 15+ messages in thread
From: Luís Mendes @ 2018-06-26 9:03 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
[-- Attachment #1.1: Type: text/plain, Size: 5215 bytes --]
I've tested Ubuntu 18.04 with kernel 4.17.2 using libdrm-2.4.92 and
mesa-18.1.0 and AMD RX 550 4GB is still hanging when running the identified
OpenCL kernels.
[ 548.704916] [drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring sdma0
timeout, last signaled seq=30, last emitted seq=33
[ 548.704988] [drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring sdma1
timeout, last signaled seq=29, last emitted seq=31
[ 548.704992] [drm] IP block:gmc_v8_0 is hung!
[ 548.704994] [drm] IP block:tonga_ih is hung!
[ 548.704996] [drm] IP block:gmc_v8_0 is hung!
[ 548.704997] [drm] IP block:gfx_v8_0 is hung!
[ 548.704998] [drm] IP block:sdma_v3_0 is hung!
[ 548.704999] [drm] IP block:tonga_ih is hung!
[ 548.705000] [drm] IP block:uvd_v6_0 is hung!
[ 548.705001] [drm] IP block:gfx_v8_0 is hung!
[ 548.705002] [drm] IP block:sdma_v3_0 is hung!
[ 548.705003] [drm] IP block:uvd_v6_0 is hung!
[ 548.705004] [drm] IP block:vce_v3_0 is hung!
[ 548.705005] [drm] GPU recovery disabled.
[ 548.705006] [drm] IP block:vce_v3_0 is hung!
[ 548.705007] [drm] GPU recovery disabled.
Are there any new regarding this issue?
Regards,
Luís
On Fri, May 25, 2018 at 11:23 AM, Luís Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
wrote:
> I've just tested Ubuntu 18.04 with kernel 4.17-rc6 using libdrm-2.4.92 and
> mesa-18.1.0.
> Now both sdma0 and sdma1 timeout as can be seen in the attached logs.
>
> ~agd5f -b drm-next-4.18 doesn't improve also.
>
> I have also tried amdgpu-pro 18.20 both on Ubuntu 18.04 and 16.04, but no
> improvements.
> I have tried amdgpu-pro 18.10 and 17.50 and also no improvements.
>
> ./amdgpu-pro-install -opencl=legacy,pal --headless
>
> On Thu, May 24, 2018 at 11:18 AM, Luís Mendes <luis.p.mendes@gmail.com>
> wrote:
>
>> Additional update...
>>
>> I was able to boot and enter X by installing an NVIDIA GTX 1050 Ti as the
>> primary display card and using an AMD RX 550 as the secondary card on the
>> Tyan S7025 with the same Ubuntu 18.04 and the same Linux kernel 4.17-rc6.
>> However once I try to run an OpenCL kernel on RX 550 I get a sdma1
>> timeout and the GPU hangs, which likely what is happening when I boot with
>> RX 550 as the single GPU card on the system.
>>
>> This means it is not an issue introduced in 4.17-rc6, it just means that
>> I didn't notice the effect of the system with the two GPUs vs system with
>> single AMD GPU.
>>
>> The dmesg log follows attached.
>>
>> Luís
>>
>> On Thu, May 24, 2018 at 10:13 AM, Luís Mendes <luis.p.mendes@gmail.com>
>> wrote:
>>
>>> Hi Michel,
>>>
>>> I also work as a researcher at a university and we are considering
>>> buying AMD cards to do OpenCL computations for numerical modelling, but
>>> currently I am unable to give a try at the AMD cards I have at home.
>>> I couldn't find any working driver for them... also amdgpu-pro drivers
>>> don't work, or at least I have been unable to make them work.
>>>
>>> Regards,
>>> Luís
>>>
>>> On Thu, May 24, 2018 at 10:01 AM, Luís Mendes <luis.p.mendes@gmail.com>
>>> wrote:
>>>
>>>> Hi Michel,
>>>>
>>>> So summarizing with Linux kernel 4.17-rc6 on Ubuntu 18.04 using AMD RX
>>>> 460/RX 550 I am not able to enter X.
>>>> The same system with AMD Radeon R7 240 not only enters X as also runs
>>>> the OpenCL kernel that RX 460 / RX 550 are unable to run for all the
>>>> kernels that I have tested.
>>>> Could this also be a Mesa issue, regarding OpenCL on RX 460?
>>>>
>>>> Regards,
>>>> Luís
>>>>
>>>> On Thu, May 24, 2018 at 9:55 AM, Luís Mendes <luis.p.mendes@gmail.com>
>>>> wrote:
>>>>
>>>>> Hi Michel,
>>>>>
>>>>> I will have to check previous rc releases of 4.17 to see if it wasn't
>>>>> already happening, before trying any possible git bisect.
>>>>> As an update I can say that an AMD Radeon R7 240 works fine on the
>>>>> same system with the same kernel and I am able to run the OpenCL kernels,
>>>>> that I couldn't with RX 460/RX 550.
>>>>>
>>>>> Regards,
>>>>> Luís
>>>>>
>>>>> On Thu, May 24, 2018 at 9:30 AM, Michel Dänzer <michel@daenzer.net>
>>>>> wrote:
>>>>>
>>>>>> On 2018-05-24 12:06 AM, Luís Mendes wrote:
>>>>>> > I've tried Linux 4.17-rc6 with Ubuntu 18.04 on Tyan S7002 and I am
>>>>>> not even
>>>>>> > able see lightdm/gdm3 as system hangs when starting X.
>>>>>> > Having SR-IOV enabled or disabled makes no difference.
>>>>>> > Tested with AMD RX 460.
>>>>>> > When X is supposed to start the system hangs and only a rectangular
>>>>>> region
>>>>>> > on the top left corner screen remains with console text messages
>>>>>> from the
>>>>>> > boot process while the remaining of the screen is just black. I am
>>>>>> unable
>>>>>> > to do anything with the keyboard, switching to console does not
>>>>>> work,
>>>>>> > ctrl-alt-del also doesn't work. I've to do a cold reset.
>>>>>>
>>>>>> Can you isolate which change introduced this new issue with git
>>>>>> bisect?
>>>>>>
>>>>>>
>>>>>> --
>>>>>> Earthling Michel Dänzer |
>>>>>> http://www.amd.com
>>>>>> Libre software enthusiast | Mesa and X
>>>>>> developer
>>>>>>
>>>>>
>>>>>
>>>>
>>>
>>
>
[-- Attachment #1.2: Type: text/html, Size: 8580 bytes --]
[-- Attachment #2: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
* Re: GPU hang trying to run OpenCL kernels on x86_64
[not found] ` <CAEzXK1oTc9p5hS97qNQHaW3Z82FXsDprSpfG4qVDhwT6VAaOhQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
@ 2018-07-10 22:06 ` Luís Mendes
0 siblings, 0 replies; 15+ messages in thread
From: Luís Mendes @ 2018-07-10 22:06 UTC (permalink / raw)
To: Michel Dänzer; +Cc: Abramov, Slava, Koenig, Christian, amd-gfx list
[-- Attachment #1.1: Type: text/plain, Size: 6525 bytes --]
Hi,
Issue remains in kernel 4.17.5, tested with SAPPHIRE RX 550 4GB running
same OpenCL kernel.
[ 227.443025] [drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring sdma0
timeout, last signaled seq=22, last emitted seq=25
[ 227.443112] [drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring sdma1
timeout, last signaled seq=22, last emitted seq=24
[ 227.443117] [drm] IP block:gmc_v8_0 is hung!
[ 227.443120] [drm] IP block:tonga_ih is hung!
[ 227.443123] [drm] IP block:gfx_v8_0 is hung!
[ 227.443124] [drm] IP block:gmc_v8_0 is hung!
[ 227.443126] [drm] IP block:tonga_ih is hung!
[ 227.443127] [drm] IP block:sdma_v3_0 is hung!
[ 227.443128] [drm] IP block:uvd_v6_0 is hung!
[ 227.443130] [drm] IP block:gfx_v8_0 is hung!
[ 227.443132] [drm] IP block:sdma_v3_0 is hung!
[ 227.443133] [drm] IP block:vce_v3_0 is hung!
[ 227.443134] [drm] GPU recovery disabled.
[ 227.443137] [drm] IP block:uvd_v6_0 is hung!
[ 227.443140] [drm] IP block:vce_v3_0 is hung!
[ 227.443141] [drm] GPU recovery disabled.
Regards,
Luís
On Tue, Jun 26, 2018 at 10:03 AM, Luís Mendes <luis.p.mendes-Re5JQEeQqe8AvxtiuMwx3w@public.gmane.org>
wrote:
>
> I've tested Ubuntu 18.04 with kernel 4.17.2 using libdrm-2.4.92 and
> mesa-18.1.0 and AMD RX 550 4GB is still hanging when running the identified
> OpenCL kernels.
>
> [ 548.704916] [drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring sdma0
> timeout, last signaled seq=30, last emitted seq=33
> [ 548.704988] [drm:amdgpu_job_timedout [amdgpu]] *ERROR* ring sdma1
> timeout, last signaled seq=29, last emitted seq=31
> [ 548.704992] [drm] IP block:gmc_v8_0 is hung!
> [ 548.704994] [drm] IP block:tonga_ih is hung!
> [ 548.704996] [drm] IP block:gmc_v8_0 is hung!
> [ 548.704997] [drm] IP block:gfx_v8_0 is hung!
> [ 548.704998] [drm] IP block:sdma_v3_0 is hung!
> [ 548.704999] [drm] IP block:tonga_ih is hung!
> [ 548.705000] [drm] IP block:uvd_v6_0 is hung!
> [ 548.705001] [drm] IP block:gfx_v8_0 is hung!
> [ 548.705002] [drm] IP block:sdma_v3_0 is hung!
> [ 548.705003] [drm] IP block:uvd_v6_0 is hung!
> [ 548.705004] [drm] IP block:vce_v3_0 is hung!
> [ 548.705005] [drm] GPU recovery disabled.
> [ 548.705006] [drm] IP block:vce_v3_0 is hung!
> [ 548.705007] [drm] GPU recovery disabled.
>
> Are there any new regarding this issue?
>
> Regards,
> Luís
>
> On Fri, May 25, 2018 at 11:23 AM, Luís Mendes <luis.p.mendes@gmail.com>
> wrote:
>
>> I've just tested Ubuntu 18.04 with kernel 4.17-rc6 using libdrm-2.4.92
>> and mesa-18.1.0.
>> Now both sdma0 and sdma1 timeout as can be seen in the attached logs.
>>
>> ~agd5f -b drm-next-4.18 doesn't improve also.
>>
>> I have also tried amdgpu-pro 18.20 both on Ubuntu 18.04 and 16.04, but no
>> improvements.
>> I have tried amdgpu-pro 18.10 and 17.50 and also no improvements.
>>
>> ./amdgpu-pro-install -opencl=legacy,pal --headless
>>
>> On Thu, May 24, 2018 at 11:18 AM, Luís Mendes <luis.p.mendes@gmail.com>
>> wrote:
>>
>>> Additional update...
>>>
>>> I was able to boot and enter X by installing an NVIDIA GTX 1050 Ti as
>>> the primary display card and using an AMD RX 550 as the secondary card on
>>> the Tyan S7025 with the same Ubuntu 18.04 and the same Linux kernel
>>> 4.17-rc6.
>>> However once I try to run an OpenCL kernel on RX 550 I get a sdma1
>>> timeout and the GPU hangs, which likely what is happening when I boot with
>>> RX 550 as the single GPU card on the system.
>>>
>>> This means it is not an issue introduced in 4.17-rc6, it just means that
>>> I didn't notice the effect of the system with the two GPUs vs system with
>>> single AMD GPU.
>>>
>>> The dmesg log follows attached.
>>>
>>> Luís
>>>
>>> On Thu, May 24, 2018 at 10:13 AM, Luís Mendes <luis.p.mendes@gmail.com>
>>> wrote:
>>>
>>>> Hi Michel,
>>>>
>>>> I also work as a researcher at a university and we are considering
>>>> buying AMD cards to do OpenCL computations for numerical modelling, but
>>>> currently I am unable to give a try at the AMD cards I have at home.
>>>> I couldn't find any working driver for them... also amdgpu-pro drivers
>>>> don't work, or at least I have been unable to make them work.
>>>>
>>>> Regards,
>>>> Luís
>>>>
>>>> On Thu, May 24, 2018 at 10:01 AM, Luís Mendes <luis.p.mendes@gmail.com>
>>>> wrote:
>>>>
>>>>> Hi Michel,
>>>>>
>>>>> So summarizing with Linux kernel 4.17-rc6 on Ubuntu 18.04 using AMD RX
>>>>> 460/RX 550 I am not able to enter X.
>>>>> The same system with AMD Radeon R7 240 not only enters X as also runs
>>>>> the OpenCL kernel that RX 460 / RX 550 are unable to run for all the
>>>>> kernels that I have tested.
>>>>> Could this also be a Mesa issue, regarding OpenCL on RX 460?
>>>>>
>>>>> Regards,
>>>>> Luís
>>>>>
>>>>> On Thu, May 24, 2018 at 9:55 AM, Luís Mendes <luis.p.mendes@gmail.com>
>>>>> wrote:
>>>>>
>>>>>> Hi Michel,
>>>>>>
>>>>>> I will have to check previous rc releases of 4.17 to see if it wasn't
>>>>>> already happening, before trying any possible git bisect.
>>>>>> As an update I can say that an AMD Radeon R7 240 works fine on the
>>>>>> same system with the same kernel and I am able to run the OpenCL kernels,
>>>>>> that I couldn't with RX 460/RX 550.
>>>>>>
>>>>>> Regards,
>>>>>> Luís
>>>>>>
>>>>>> On Thu, May 24, 2018 at 9:30 AM, Michel Dänzer <michel@daenzer.net>
>>>>>> wrote:
>>>>>>
>>>>>>> On 2018-05-24 12:06 AM, Luís Mendes wrote:
>>>>>>> > I've tried Linux 4.17-rc6 with Ubuntu 18.04 on Tyan S7002 and I am
>>>>>>> not even
>>>>>>> > able see lightdm/gdm3 as system hangs when starting X.
>>>>>>> > Having SR-IOV enabled or disabled makes no difference.
>>>>>>> > Tested with AMD RX 460.
>>>>>>> > When X is supposed to start the system hangs and only a
>>>>>>> rectangular region
>>>>>>> > on the top left corner screen remains with console text messages
>>>>>>> from the
>>>>>>> > boot process while the remaining of the screen is just black. I am
>>>>>>> unable
>>>>>>> > to do anything with the keyboard, switching to console does not
>>>>>>> work,
>>>>>>> > ctrl-alt-del also doesn't work. I've to do a cold reset.
>>>>>>>
>>>>>>> Can you isolate which change introduced this new issue with git
>>>>>>> bisect?
>>>>>>>
>>>>>>>
>>>>>>> --
>>>>>>> Earthling Michel Dänzer |
>>>>>>> http://www.amd.com
>>>>>>> Libre software enthusiast | Mesa and X
>>>>>>> developer
>>>>>>>
>>>>>>
>>>>>>
>>>>>
>>>>
>>>
>>
>
[-- Attachment #1.2: Type: text/html, Size: 10473 bytes --]
[-- Attachment #2: Type: text/plain, Size: 154 bytes --]
_______________________________________________
amd-gfx mailing list
amd-gfx@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/amd-gfx
^ permalink raw reply [flat|nested] 15+ messages in thread
end of thread, other threads:[~2018-07-10 22:06 UTC | newest]
Thread overview: 15+ messages (download: mbox.gz / follow: Atom feed)
-- links below jump to the message on this page --
2018-05-04 16:27 GPU hang trying to run OpenCL kernels on x86_64 Luís Mendes
[not found] ` <CAEzXK1p3SnOnduP0nL1D1pNWH1LTWwApEs7QnQPTFDdBBiHLXA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-05-04 18:18 ` Abramov, Slava
[not found] ` <CY4PR12MB13045EA9BCBFAB20D698BA86FE860-rpdhrqHFk05fmUFYn07qFQdYzm3356FpvxpqHgZTriW3zl9H0oFU5g@public.gmane.org>
2018-05-04 23:15 ` Luís Mendes
[not found] ` <CAEzXK1rJbXSpLUm=XQTLvySM4HJ45G9fQ0WCTPhnvdPETwUaYA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-05-07 9:38 ` Michel Dänzer
[not found] ` <53cc38f2-e94a-1514-0a03-303101db2f88-otUistvHUpPR7s880joybQ@public.gmane.org>
2018-05-07 12:31 ` Luís Mendes
[not found] ` <CAEzXK1qHtfOBgismLvNy_x+NcMw78288AuwovBR-JmRwqpDmGQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-05-11 12:15 ` Luís Mendes
[not found] ` <CAEzXK1oM6b1bV3R3ezwD4eYrJXWV9+cdUFMC4q5+1bPkpmJFqQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-05-23 22:06 ` Luís Mendes
[not found] ` <CAEzXK1qRWkL67rG40jk4Odqm8AjbDvnnaCsDycLPRcPXXPL-KQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-05-24 8:30 ` Michel Dänzer
[not found] ` <22178876-688c-b4fe-d40e-1bab28024603-otUistvHUpPR7s880joybQ@public.gmane.org>
2018-05-24 8:55 ` Luís Mendes
[not found] ` <CAEzXK1q+pMZgg7a7TMkNaDPhe90NkCc7MtAfE98vRY5tGDfW4A-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-05-24 9:01 ` Luís Mendes
[not found] ` <CAEzXK1pZqFMZ8Qos3h7E-aYdmBE18GKFSamPV+0ZsXu=CatKRA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-05-24 9:13 ` Luís Mendes
[not found] ` <CAEzXK1qtjy+OaBh5rkzOXrTYe4Zq1w5bzdzTSRuCuDcm-kx-fA-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-05-24 10:18 ` Luís Mendes
[not found] ` <CAEzXK1ryiqqrxTr5mn+Y4VvNAn-LtQb-0cBTitKKoQb+4B1=Qg-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-05-25 10:23 ` Luís Mendes
[not found] ` <CAEzXK1ob33a28y_jwj_8ovr_ZDiowMAiUrnAQxS4vM5PK3NzzQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-06-26 9:03 ` Luís Mendes
[not found] ` <CAEzXK1oTc9p5hS97qNQHaW3Z82FXsDprSpfG4qVDhwT6VAaOhQ-JsoAwUIsXosN+BqQ9rBEUg@public.gmane.org>
2018-07-10 22:06 ` Luís Mendes
This is an external index of several public inboxes,
see mirroring instructions on how to clone and mirror
all data and code used by this external index.