Hi,
On performing simultaneous capturing of images from three cameras sensors on NX module, infrequently we see the capture failing for one of the sensor and gradually all camera capture fails. v4l2 throws V4L2_BUF_FLAG_ERROR, when this happens. We are using v4l2+ userspace + memory allocated via cudaMallocManaged(…) for the capture.
We are unsure of the where the issue is. Please provide pointers to debug this issue
Further details are as follows
Tried following and still did not help
- Adding serdes_pix_clk_hz = “833333333” to dts file
- Push clock to maximum
cat /sys/kernel/debug/bpmp/debug/clk/nvcsi/rate ==> 314000000
cat /sys/kernel/debug/bpmp/debug/clk/vi/rate ==> 460800000
System details:
- R32.4.3
- Kernel version 4.9.140-tegra
Below is the DTS that is being used
mode0 { mclk_khz = "74250"; num_lanes = "4"; tegra_sinterface = "serial_c"; phy_mode = "DPHY"; discontinuous_clk = "yes"; dpcm_enable = "false"; cil_settletime = "0"; active_w = "1472"; //1440+32 active_h = "1080"; mode_type = "bayer"; pixel_phase = "bggr"; csi_pixel_bit_depth = "10"; readout_orientation = "0"; line_length = "1856"; inherent_gain = "1"; mclk_multiplier = "6.4"; //"12.53"; pix_clk_hz = "475201702"; //"465061632"; //1130x1856x226.58 gain_factor = "16"; framerate_factor = "1000000"; exposure_factor = "1000000"; min_gain_val = "0"; max_gain_val = "48"; step_gain_val = "1"; default_gain = "48"; min_hdr_ratio = "1"; max_hdr_ratio = "1"; min_framerate = "2000000"; /* 2.0 fps */ max_framerate = "226580000"; /* 226.5 fps */ step_framerate = "1"; default_framerate = "226580000"; /* 226.5 fps */ min_exp_time = "1"; /* us */ max_exp_time = "100000"; /* us */ step_exp_time = "1"; default_exp_time = "100"; /* us */ embedded_metadata_height = "0"; };
Following are the trace logs.
vi-output, imx2-6002 [001] … 464.220947: tegra_channel_capture_frame: eof:474.709343616
vi-output, imx2-6002 [001] … 464.239520: tegra_channel_capture_frame: sof:474.722082880
vi-output, imx2-6002 [001] … 464.239521: tegra_channel_capture_frame: eof:474.726303680
vi-output, imx2-6002 [001] … 464.239682: tegra_channel_capture_frame: sof:474.727042976
vi-output, imx2-6002 [001] … 464.239682: tegra_channel_capture_frame: eof:474.731263744CPU 0 buffer started
kworker/0:1-787 [000] .... 464.246924: rtcpu_nvcsi_intr: tstamp:14833916154 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246924: rtcpu_nvcsi_intr: tstamp:14833917443 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246924: rtcpu_nvcsi_intr: tstamp:14833917443 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246925: rtcpu_nvcsi_intr: tstamp:14833917443 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246925: rtcpu_nvcsi_intr: tstamp:14833917443 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246925: rtcpu_nvcsi_intr: tstamp:14833917443 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246925: rtcpu_nvcsi_intr: tstamp:14833917443 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246925: rtcpu_nvcsi_intr: tstamp:14833918779 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246925: rtcpu_nvcsi_intr: tstamp:14833918779 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246926: rtcpu_nvcsi_intr: tstamp:14833918779 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246926: rtcpu_nvcsi_intr: tstamp:14833918779 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246926: rtcpu_nvcsi_intr: tstamp:14833918779 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246926: rtcpu_nvcsi_intr: tstamp:14833918779 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246926: rtcpu_nvcsi_intr: tstamp:14833920074 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246926: rtcpu_nvcsi_intr: tstamp:14833920074 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246926: rtcpu_nvcsi_intr: tstamp:14833920074 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246927: rtcpu_nvcsi_intr: tstamp:14833920074 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246927: rtcpu_nvcsi_intr: tstamp:14833920074 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246927: rtcpu_nvcsi_intr: tstamp:14833920074 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246927: rtcpu_nvcsi_intr: tstamp:14833921367 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246927: rtcpu_nvcsi_intr: tstamp:14833921367 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246927: rtcpu_nvcsi_intr: tstamp:14833921367 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246927: rtcpu_nvcsi_intr: tstamp:14833921367 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246928: rtcpu_nvcsi_intr: tstamp:14833921367 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246928: rtcpu_nvcsi_intr: tstamp:14833921367 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246928: rtcpu_nvcsi_intr: tstamp:14833922666 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246928: rtcpu_nvcsi_intr: tstamp:14833922666 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246928: rtcpu_nvcsi_intr: tstamp:14833922666 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246928: rtcpu_nvcsi_intr: tstamp:14833922666 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246929: rtcpu_nvcsi_intr: tstamp:14833922666 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246929: rtcpu_nvcsi_intr: tstamp:14833922666 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246929: rtcpu_nvcsi_intr: tstamp:14833923959 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246929: rtcpu_nvcsi_intr: tstamp:14833923959 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246929: rtcpu_nvcsi_intr: tstamp:14833923959 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246929: rtcpu_nvcsi_intr: tstamp:14833923959 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246930: rtcpu_nvcsi_intr: tstamp:14833923959 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246930: rtcpu_nvcsi_intr: tstamp:14833923959 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246930: rtcpu_nvcsi_intr: tstamp:14833925249 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246930: rtcpu_nvcsi_intr: tstamp:14833925249 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246930: rtcpu_nvcsi_intr: tstamp:14833925249 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246930: rtcpu_nvcsi_intr: tstamp:14833925249 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246930: rtcpu_nvcsi_intr: tstamp:14833925249 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246931: rtcpu_nvcsi_intr: tstamp:14833925249 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246931: rtcpu_nvcsi_intr: tstamp:14833926547 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246931: rtcpu_nvcsi_intr: tstamp:14833926547 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246931: rtcpu_nvcsi_intr: tstamp:14833926547 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246931: rtcpu_nvcsi_intr: tstamp:14833926547 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246931: rtcpu_nvcsi_intr: tstamp:14833926547 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246931: rtcpu_nvcsi_intr: tstamp:14833926547 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246932: rtcpu_nvcsi_intr: tstamp:14833927840 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246932: rtcpu_nvcsi_intr: tstamp:14833927840 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246932: rtcpu_nvcsi_intr: tstamp:14833927840 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246932: rtcpu_nvcsi_intr: tstamp:14833927840 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246932: rtcpu_nvcsi_intr: tstamp:14833927840 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246932: rtcpu_nvcsi_intr: tstamp:14833927840 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246933: rtcpu_nvcsi_intr: tstamp:14833929134 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246933: rtcpu_nvcsi_intr: tstamp:14833929134 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246933: rtcpu_nvcsi_intr: tstamp:14833929134 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246933: rtcpu_nvcsi_intr: tstamp:14833929134 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246933: rtcpu_nvcsi_intr: tstamp:14833929134 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246933: rtcpu_nvcsi_intr: tstamp:14833929134 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246933: rtcpu_nvcsi_intr: tstamp:14833930428 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246934: rtcpu_nvcsi_intr: tstamp:14833930428 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246934: rtcpu_nvcsi_intr: tstamp:14833930428 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246934: rtcpu_nvcsi_intr: tstamp:14833930428 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246934: rtcpu_nvcsi_intr: tstamp:14833930428 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246934: rtcpu_nvcsi_intr: tstamp:14833930428 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246934: rtcpu_nvcsi_intr: tstamp:14833931722 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246935: rtcpu_nvcsi_intr: tstamp:14833931722 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246935: rtcpu_nvcsi_intr: tstamp:14833931722 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246935: rtcpu_nvcsi_intr: tstamp:14833931722 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246935: rtcpu_nvcsi_intr: tstamp:14833931722 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246935: rtcpu_nvcsi_intr: tstamp:14833931722 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246935: rtcpu_nvcsi_intr: tstamp:14833933025 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246935: rtcpu_nvcsi_intr: tstamp:14833933025 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246936: rtcpu_nvcsi_intr: tstamp:14833933025 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246936: rtcpu_nvcsi_intr: tstamp:14833933025 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246936: rtcpu_nvcsi_intr: tstamp:14833933025 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246936: rtcpu_nvcsi_intr: tstamp:14833933025 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246936: rtcpu_nvcsi_intr: tstamp:14833934318 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246936: rtcpu_nvcsi_intr: tstamp:14833934318 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246937: rtcpu_nvcsi_intr: tstamp:14833934318 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246937: rtcpu_nvcsi_intr: tstamp:14833934318 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246937: rtcpu_nvcsi_intr: tstamp:14833934318 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246937: rtcpu_nvcsi_intr: tstamp:14833934318 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246937: rtcpu_nvcsi_intr: tstamp:14833935616 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246937: rtcpu_nvcsi_intr: tstamp:14833935616 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246937: rtcpu_nvcsi_intr: tstamp:14833935616 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246938: rtcpu_nvcsi_intr: tstamp:14833935616 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246938: rtcpu_nvcsi_intr: tstamp:14833935616 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246938: rtcpu_nvcsi_intr: tstamp:14833935616 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246938: rtcpu_nvcsi_intr: tstamp:14833936918 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246938: rtcpu_nvcsi_intr: tstamp:14833936918 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246938: rtcpu_nvcsi_intr: tstamp:14833936918 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246938: rtcpu_nvcsi_intr: tstamp:14833936918 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246939: rtcpu_nvcsi_intr: tstamp:14833936918 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246939: rtcpu_nvcsi_intr: tstamp:14833936918 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246939: rtcpu_nvcsi_intr: tstamp:14833938221 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246939: rtcpu_nvcsi_intr: tstamp:14833938221 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246939: rtcpu_nvcsi_intr: tstamp:14833938221 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246939: rtcpu_nvcsi_intr: tstamp:14833938221 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246940: rtcpu_nvcsi_intr: tstamp:14833938221 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246940: rtcpu_nvcsi_intr: tstamp:14833938221 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246940: rtcpu_nvcsi_intr: tstamp:14833939527 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246940: rtcpu_nvcsi_intr: tstamp:14833939527 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246940: rtcpu_nvcsi_intr: tstamp:14833939527 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246940: rtcpu_nvcsi_intr: tstamp:14833939527 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246940: rtcpu_nvcsi_intr: tstamp:14833939527 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246941: rtcpu_nvcsi_intr: tstamp:14833939527 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246941: rtcpu_nvcsi_intr: tstamp:14833940825 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246941: rtcpu_nvcsi_intr: tstamp:14833940825 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246941: rtcpu_nvcsi_intr: tstamp:14833940825 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246941: rtcpu_nvcsi_intr: tstamp:14833940825 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246942: rtcpu_nvcsi_intr: tstamp:14833940825 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246942: rtcpu_nvcsi_intr: tstamp:14833940825 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246942: rtcpu_nvcsi_intr: tstamp:14833942119 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246943: rtcpu_nvcsi_intr: tstamp:14833942119 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246943: rtcpu_nvcsi_intr: tstamp:14833942119 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246943: rtcpu_nvcsi_intr: tstamp:14833942119 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246943: rtcpu_nvcsi_intr: tstamp:14833942119 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246943: rtcpu_nvcsi_intr: tstamp:14833942119 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246943: rtcpu_nvcsi_intr: tstamp:14833943413 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246943: rtcpu_nvcsi_intr: tstamp:14833943413 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246944: rtcpu_nvcsi_intr: tstamp:14833943413 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246944: rtcpu_nvcsi_intr: tstamp:14833943413 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246944: rtcpu_nvcsi_intr: tstamp:14833943413 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246944: rtcpu_nvcsi_intr: tstamp:14833943413 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246944: rtcpu_nvcsi_intr: tstamp:14833944703 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246944: rtcpu_nvcsi_intr: tstamp:14833944703 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246945: rtcpu_nvcsi_intr: tstamp:14833944703 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246945: rtcpu_nvcsi_intr: tstamp:14833944703 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246945: rtcpu_nvcsi_intr: tstamp:14833944703 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246945: rtcpu_nvcsi_intr: tstamp:14833944703 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246945: rtcpu_nvcsi_intr: tstamp:14833945992 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246945: rtcpu_nvcsi_intr: tstamp:14833945992 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246945: rtcpu_nvcsi_intr: tstamp:14833945992 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246946: rtcpu_nvcsi_intr: tstamp:14833945992 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246946: rtcpu_nvcsi_intr: tstamp:14833945992 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246946: rtcpu_nvcsi_intr: tstamp:14833945992 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246946: rtcpu_nvcsi_intr: tstamp:14833947286 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246946: rtcpu_nvcsi_intr: tstamp:14833947286 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246946: rtcpu_nvcsi_intr: tstamp:14833947286 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246947: rtcpu_nvcsi_intr: tstamp:14833947286 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246947: rtcpu_nvcsi_intr: tstamp:14833947286 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246947: rtcpu_nvcsi_intr: tstamp:14833947286 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246947: rtcpu_nvcsi_intr: tstamp:14833948583 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000006 kworker/0:1-787 [000] .... 464.246947: rtcpu_nvcsi_intr: tstamp:14833948583 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246947: rtcpu_nvcsi_intr: tstamp:14833948583 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246947: rtcpu_nvcsi_intr: tstamp:14833948583 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000006 kworker/0:1-787 [000] .... 464.246948: rtcpu_vinotify_error: tstamp:14833951228 tag:CSIMUX_FRAME channel:0x00 frame:1793 vi_tstamp:14833948276 data:0x00400260 kworker/0:1-787 [000] .... 464.246949: rtcpu_vinotify_event: tstamp:14833951700 tag:CSIMUX_FRAME channel:0x00 frame:1794 vi_tstamp:14833793276 data:0x00400260 kworker/0:1-787 [000] .... 464.246949: rtcpu_vinotify_event: tstamp:14833951842 tag:CHANSEL_SHORT_FRAME channel:0x01 frame:1794 vi_tstamp:14833793276 data:0x01000000 kworker/0:1-787 [000] .... 464.246949: rtcpu_vinotify_event: tstamp:14833952009 tag:RESERVED_19 channel:0x23 frame:2 vi_tstamp:15119901952 data:0x01021fce kworker/0:1-787 [000] .... 464.246949: rtcpu_vinotify_event: tstamp:14833952148 tag:FS channel:0x00 frame:1 vi_tstamp:14833793277 data:0x00000014 kworker/0:1-787 [000] .... 464.246950: rtcpu_vinotify_event: tstamp:14833952312 tag:ATOMP_FE channel:0x00 frame:1794 vi_tstamp:14833793277 data:0x00000000 kworker/0:1-787 [000] .... 464.246950: rtcpu_vinotify_event: tstamp:14833952448 tag:RESERVED_19 channel:0x23 frame:0 vi_tstamp:15119911680 data:0x07021fcf kworker/0:1-787 [000] .... 464.246950: rtcpu_vinotify_event: tstamp:14833952612 tag:ATOMP_FS channel:0x00 frame:1 vi_tstamp:14833793278 data:0x00000000 kworker/0:1-787 [000] .... 464.246950: rtcpu_vinotify_event: tstamp:14833952748 tag:RESERVED_18 channel:0x23 frame:0 vi_tstamp:15120138912 data:0x10000000 kworker/0:1-787 [000] .... 464.246950: rtcpu_vinotify_event: tstamp:14833952906 tag:RESERVED_18 channel:0x23 frame:0 vi_tstamp:15120147552 data:0x31001fd0 kworker/0:1-787 [000] .... 464.246950: rtcpu_vinotify_event: tstamp:14833953041 tag:FS channel:0x00 frame:1793 vi_tstamp:14833816349 data:0x00000010 kworker/0:1-787 [000] .... 464.246950: rtcpu_vinotify_event: tstamp:14833953195 tag:ATOMP_FS channel:0x00 frame:1793 vi_tstamp:14833816349 data:0x00000000 kworker/0:1-787 [000] .... 464.246951: rtcpu_vinotify_event: tstamp:14833953330 tag:CHANSEL_PXL_SOF channel:0x22 frame:1 vi_tstamp:14833816351 data:0x00000001 kworker/0:1-787 [000] .... 464.246951: rtcpu_vinotify_event: tstamp:14833953487 tag:RESERVED_19 channel:0x22 frame:1 vi_tstamp:15120626784 data:0x08021947 kworker/0:1-787 [000] .... 464.246951: rtcpu_vinotify_event: tstamp:14833953621 tag:CHANSEL_PXL_SOF channel:0x23 frame:1793 vi_tstamp:14833816473 data:0x00000001 kworker/0:1-787 [000] .... 464.246951: rtcpu_vinotify_event: tstamp:14833953779 tag:RESERVED_19 channel:0x23 frame:1 vi_tstamp:15120632608 data:0x08021fcf kworker/0:1-787 [000] .... 464.246951: rtcpu_vinotify_event: tstamp:14833953912 tag:FE channel:0x00 frame:1 vi_tstamp:14833826981 data:0x00000022 kworker/0:1-787 [000] .... 464.246951: rtcpu_vinotify_event: tstamp:14833954068 tag:FS channel:0x00 frame:2 vi_tstamp:14833827008 data:0x00000012 kworker/0:1-787 [000] .... 464.246952: rtcpu_vinotify_event: tstamp:14833954204 tag:ATOMP_FS channel:0x00 frame:2 vi_tstamp:14833827008 data:0x00000000 kworker/0:1-787 [000] .... 464.246952: rtcpu_vinotify_event: tstamp:14833954361 tag:CHANSEL_PXL_SOF channel:0x21 frame:2 vi_tstamp:14833850085 data:0x00000001 kworker/0:1-787 [000] .... 464.246952: rtcpu_vinotify_event: tstamp:14833954496 tag:RESERVED_19 channel:0x21 frame:2 vi_tstamp:15121703104 data:0x08021940 kworker/0:1-787 [000] .... 464.246952: rtcpu_vinotify_event: tstamp:14833954651 tag:CHANSEL_PXL_EOF channel:0x22 frame:1 vi_tstamp:14833948142 data:0x04370002 kworker/0:1-787 [000] .... 464.246952: rtcpu_vinotify_event: tstamp:14833954786 tag:ATOMP_FRAME_DONE channel:0x22 frame:1 vi_tstamp:14833948171 data:0x00000000 kworker/0:1-787 [000] .... 464.246952: rtcpu_vinotify_event: tstamp:14833954943 tag:RESERVED_19 channel:0x22 frame:1 vi_tstamp:15124841888 data:0x02021947 kworker/0:1-787 [000] .... 464.246953: rtcpu_vinotify_event: tstamp:14833955077 tag:FE channel:0x00 frame:1 vi_tstamp:14833948250 data:0x00000024 kworker/0:1-787 [000] .... 464.246953: rtcpu_vinotify_event: tstamp:14833955232 tag:ATOMP_FE channel:0x00 frame:1 vi_tstamp:14833948250 data:0x00000000 kworker/0:1-787 [000] .... 464.246953: rtcpu_vinotify_event: tstamp:14833955369 tag:RESERVED_19 channel:0x22 frame:1 vi_tstamp:15124848160 data:0x00021947 kworker/0:1-787 [000] .... 464.246953: rtcpu_vinotify_event: tstamp:14833955525 tag:CSIMUX_FRAME channel:0x00 frame:1793 vi_tstamp:14833948276 data:0x00400260 kworker/0:1-787 [000] .... 464.246953: rtcpu_vinotify_event: tstamp:14833955664 tag:CHANSEL_SHORT_FRAME channel:0x01 frame:1793 vi_tstamp:14833948276 data:0x01000000 kworker/0:1-787 [000] .... 464.246953: rtcpu_vinotify_event: tstamp:14833955822 tag:RESERVED_19 channel:0x23 frame:1 vi_tstamp:15124859296 data:0x01021fcf kworker/0:1-787 [000] .... 464.246954: rtcpu_vinotify_event: tstamp:14833955958 tag:ATOMP_FE channel:0x00 frame:1793 vi_tstamp:14833948276 data:0x00000000 kworker/0:1-787 [000] .... 464.246954: rtcpu_vinotify_event: tstamp:14833956114 tag:RESERVED_19 channel:0x23 frame:0 vi_tstamp:15124868416 data:0x07021fd0 kworker/0:1-787 [000] .... 464.246954: rtcpu_vinotify_event: tstamp:14833956248 tag:FS channel:0x00 frame:2 vi_tstamp:14833948276 data:0x00000014 kworker/0:1-787 [000] .... 464.246957: rtcpu_nvcsi_intr: tstamp:14833971429 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000002 kworker/0:1-787 [000] .... 464.246957: rtcpu_nvcsi_intr: tstamp:14833971429 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246957: rtcpu_nvcsi_intr: tstamp:14833971429 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000006 kworker/0:1-787 [000] .... 464.246957: rtcpu_nvcsi_intr: tstamp:14833971429 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246957: rtcpu_nvcsi_intr: tstamp:14833971429 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246957: rtcpu_nvcsi_intr: tstamp:14833972601 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246958: rtcpu_nvcsi_intr: tstamp:14833972601 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246958: rtcpu_nvcsi_intr: tstamp:14833972601 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246958: rtcpu_nvcsi_intr: tstamp:14833972601 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246958: rtcpu_nvcsi_intr: tstamp:14833972601 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246958: rtcpu_nvcsi_intr: tstamp:14833972601 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246958: rtcpu_nvcsi_intr: tstamp:14833973902 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246959: rtcpu_nvcsi_intr: tstamp:14833973902 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246959: rtcpu_nvcsi_intr: tstamp:14833973902 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246959: rtcpu_nvcsi_intr: tstamp:14833973902 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246959: rtcpu_nvcsi_intr: tstamp:14833973902 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246959: rtcpu_nvcsi_intr: tstamp:14833973902 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246959: rtcpu_nvcsi_intr: tstamp:14833975195 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246959: rtcpu_nvcsi_intr: tstamp:14833975195 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246960: rtcpu_nvcsi_intr: tstamp:14833975195 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246960: rtcpu_nvcsi_intr: tstamp:14833975195 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246960: rtcpu_nvcsi_intr: tstamp:14833975195 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246960: rtcpu_nvcsi_intr: tstamp:14833975195 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246960: rtcpu_nvcsi_intr: tstamp:14833976490 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246960: rtcpu_nvcsi_intr: tstamp:14833976490 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246961: rtcpu_nvcsi_intr: tstamp:14833976490 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246961: rtcpu_nvcsi_intr: tstamp:14833976490 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246961: rtcpu_nvcsi_intr: tstamp:14833976490 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246961: rtcpu_nvcsi_intr: tstamp:14833976490 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246961: rtcpu_nvcsi_intr: tstamp:14833977784 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246961: rtcpu_nvcsi_intr: tstamp:14833977784 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246962: rtcpu_nvcsi_intr: tstamp:14833977784 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246962: rtcpu_nvcsi_intr: tstamp:14833977784 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246962: rtcpu_nvcsi_intr: tstamp:14833977784 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246962: rtcpu_nvcsi_intr: tstamp:14833977784 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246962: rtcpu_nvcsi_intr: tstamp:14833979082 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246962: rtcpu_nvcsi_intr: tstamp:14833979082 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246963: rtcpu_nvcsi_intr: tstamp:14833979082 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246963: rtcpu_nvcsi_intr: tstamp:14833979082 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246963: rtcpu_nvcsi_intr: tstamp:14833979082 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246964: rtcpu_nvcsi_intr: tstamp:14833979082 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246964: rtcpu_nvcsi_intr: tstamp:14833980376 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246964: rtcpu_nvcsi_intr: tstamp:14833980376 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246964: rtcpu_nvcsi_intr: tstamp:14833980376 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246964: rtcpu_nvcsi_intr: tstamp:14833980376 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246964: rtcpu_nvcsi_intr: tstamp:14833980376 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246965: rtcpu_nvcsi_intr: tstamp:14833980376 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246965: rtcpu_nvcsi_intr: tstamp:14833981707 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246965: rtcpu_nvcsi_intr: tstamp:14833981707 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246965: rtcpu_nvcsi_intr: tstamp:14833981707 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246965: rtcpu_nvcsi_intr: tstamp:14833981707 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246965: rtcpu_nvcsi_intr: tstamp:14833981707 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246966: rtcpu_nvcsi_intr: tstamp:14833981707 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246966: rtcpu_nvcsi_intr: tstamp:14833982998 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246966: rtcpu_nvcsi_intr: tstamp:14833982998 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246966: rtcpu_nvcsi_intr: tstamp:14833982998 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246966: rtcpu_nvcsi_intr: tstamp:14833982998 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246966: rtcpu_nvcsi_intr: tstamp:14833982998 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246966: rtcpu_nvcsi_intr: tstamp:14833982998 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246967: rtcpu_nvcsi_intr: tstamp:14833984288 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246967: rtcpu_nvcsi_intr: tstamp:14833984288 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246967: rtcpu_nvcsi_intr: tstamp:14833984288 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246967: rtcpu_nvcsi_intr: tstamp:14833984288 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246967: rtcpu_nvcsi_intr: tstamp:14833984288 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246967: rtcpu_nvcsi_intr: tstamp:14833984288 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246968: rtcpu_nvcsi_intr: tstamp:14833985577 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246968: rtcpu_nvcsi_intr: tstamp:14833985577 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246968: rtcpu_nvcsi_intr: tstamp:14833985577 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246968: rtcpu_nvcsi_intr: tstamp:14833985577 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246968: rtcpu_nvcsi_intr: tstamp:14833985577 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246968: rtcpu_nvcsi_intr: tstamp:14833985577 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246968: rtcpu_nvcsi_intr: tstamp:14833986875 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246969: rtcpu_nvcsi_intr: tstamp:14833986875 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246969: rtcpu_nvcsi_intr: tstamp:14833986875 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246969: rtcpu_nvcsi_intr: tstamp:14833986875 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246969: rtcpu_nvcsi_intr: tstamp:14833986875 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246969: rtcpu_nvcsi_intr: tstamp:14833986875 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246969: rtcpu_nvcsi_intr: tstamp:14833988171 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246970: rtcpu_nvcsi_intr: tstamp:14833988171 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246970: rtcpu_nvcsi_intr: tstamp:14833988171 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246970: rtcpu_nvcsi_intr: tstamp:14833988171 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246970: rtcpu_nvcsi_intr: tstamp:14833988171 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246970: rtcpu_nvcsi_intr: tstamp:14833988171 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246970: rtcpu_nvcsi_intr: tstamp:14833989467 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246970: rtcpu_nvcsi_intr: tstamp:14833989467 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246971: rtcpu_nvcsi_intr: tstamp:14833989467 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246971: rtcpu_nvcsi_intr: tstamp:14833989467 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246971: rtcpu_nvcsi_intr: tstamp:14833989467 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246971: rtcpu_nvcsi_intr: tstamp:14833989467 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246971: rtcpu_nvcsi_intr: tstamp:14833990760 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246971: rtcpu_nvcsi_intr: tstamp:14833990760 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246971: rtcpu_nvcsi_intr: tstamp:14833990760 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246972: rtcpu_nvcsi_intr: tstamp:14833990760 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246972: rtcpu_nvcsi_intr: tstamp:14833990760 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246972: rtcpu_nvcsi_intr: tstamp:14833990760 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246972: rtcpu_nvcsi_intr: tstamp:14833992049 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246972: rtcpu_nvcsi_intr: tstamp:14833992049 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246972: rtcpu_nvcsi_intr: tstamp:14833992049 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246973: rtcpu_nvcsi_intr: tstamp:14833992049 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246973: rtcpu_nvcsi_intr: tstamp:14833992049 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246973: rtcpu_nvcsi_intr: tstamp:14833992049 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246973: rtcpu_nvcsi_intr: tstamp:14833993346 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246973: rtcpu_nvcsi_intr: tstamp:14833993346 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246973: rtcpu_nvcsi_intr: tstamp:14833993346 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246973: rtcpu_nvcsi_intr: tstamp:14833993346 class:CORRECTABLE_ERR type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246974: rtcpu_nvcsi_intr: tstamp:14833993346 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246974: rtcpu_nvcsi_intr: tstamp:14833993346 class:CORRECTABLE_ERR type:PHY_INTR phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246974: rtcpu_nvcsi_intr: tstamp:14833994638 class:GLOBAL type:STREAM_VC phy:0 cil:0 st:0 vc:0 status:0x00000004 kworker/0:1-787 [000] .... 464.246974: rtcpu_nvcsi_intr: tstamp:14833994638 class:GLOBAL type:PHY_INTR0 phy:0 cil:0 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] .... 464.246974: rtcpu_nvcsi_intr: tstamp:14833994638 class:GLOBAL type:PHY_INTR0 phy:0 cil:1 st:0 vc:0 status:0x00000110 kworker/0:1-787 [000] ....