drivers/gpu/drm/etnaviv/etnaviv_dump.c

94

reg->value = cpu_to_le32(gpu_read(gpu, read_addr));

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

1095

u32 read0 = gpu_read(gpu, VIVS_MC_DEBUG_READ0);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

1096

u32 read1 = gpu_read(gpu, VIVS_MC_DEBUG_READ1);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

1097

u32 write = gpu_read(gpu, VIVS_MC_DEBUG_WRITE);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

1477

u32 addr = gpu_read(gpu, VIVS_FE_DMA_ADDRESS);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

1549

status = gpu_read(gpu, status_reg);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

1571

i, reason, gpu_read(gpu, address_reg));

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

1580

u32 intr = gpu_read(gpu, VIVS_HI_INTR_ACKNOWLEDGE);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

1691

u32 idle = gpu_read(gpu, VIVS_HI_IDLE_STATE);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

1996

idle = gpu_read(gpu, VIVS_HI_IDLE_STATE) & mask;

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

218

specs[0] = gpu_read(gpu, VIVS_HI_CHIP_SPECS);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

219

specs[1] = gpu_read(gpu, VIVS_HI_CHIP_SPECS_2);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

220

specs[2] = gpu_read(gpu, VIVS_HI_CHIP_SPECS_3);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

221

specs[3] = gpu_read(gpu, VIVS_HI_CHIP_SPECS_4);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

365

chipIdentity = gpu_read(gpu, VIVS_HI_CHIP_IDENTITY);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

373

u32 chipDate = gpu_read(gpu, VIVS_HI_CHIP_DATE);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

375

gpu->identity.model = gpu_read(gpu, VIVS_HI_CHIP_MODEL);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

376

gpu->identity.revision = gpu_read(gpu, VIVS_HI_CHIP_REV);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

377

gpu->identity.customer_id = gpu_read(gpu, VIVS_HI_CHIP_CUSTOMER_ID);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

384

gpu->identity.product_id = gpu_read(gpu, VIVS_HI_CHIP_PRODUCT_ID);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

385

gpu->identity.eco_id = gpu_read(gpu, VIVS_HI_CHIP_ECO_ID);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

401

u32 chipTime = gpu_read(gpu, VIVS_HI_CHIP_TIME);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

442

gpu->identity.features = gpu_read(gpu, VIVS_HI_CHIP_FEATURE);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

471

gpu_read(gpu, VIVS_HI_CHIP_MINOR_FEATURE_0);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

476

gpu_read(gpu, VIVS_HI_CHIP_MINOR_FEATURE_1);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

478

gpu_read(gpu, VIVS_HI_CHIP_MINOR_FEATURE_2);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

480

gpu_read(gpu, VIVS_HI_CHIP_MINOR_FEATURE_3);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

482

gpu_read(gpu, VIVS_HI_CHIP_MINOR_FEATURE_4);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

484

gpu_read(gpu, VIVS_HI_CHIP_MINOR_FEATURE_5);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

519

u32 clock = gpu_read(gpu, VIVS_HI_CLOCK_CONTROL);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

586

idle = gpu_read(gpu, VIVS_HI_IDLE_STATE);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

595

control = gpu_read(gpu, VIVS_HI_CLOCK_CONTROL);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

613

idle = gpu_read(gpu, VIVS_HI_IDLE_STATE);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

614

control = gpu_read(gpu, VIVS_HI_CLOCK_CONTROL);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

769

gpu_read(gpu, VIVS_HI_CHIP_TIME) != 0x2062400) {

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

772

mc_memory_debug = gpu_read(gpu, VIVS_MC_DEBUG_MEMORY) & ~0xff;

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

795

u32 bus_config = gpu_read(gpu, VIVS_MC_BUS_CONFIG);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

804

u32 val = gpu_read(gpu, VIVS_MMUv2_AHB_CONTROL);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

955

debug->address[0] = gpu_read(gpu, VIVS_FE_DMA_ADDRESS);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

956

debug->state[0] = gpu_read(gpu, VIVS_FE_DMA_DEBUG_STATE);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

959

debug->address[1] = gpu_read(gpu, VIVS_FE_DMA_ADDRESS);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

960

debug->state[1] = gpu_read(gpu, VIVS_FE_DMA_DEBUG_STATE);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

982

dma_lo = gpu_read(gpu, VIVS_FE_DMA_LOW);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

983

dma_hi = gpu_read(gpu, VIVS_FE_DMA_HIGH);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

984

axi = gpu_read(gpu, VIVS_HI_AXI_STATUS);

drivers/gpu/drm/etnaviv/etnaviv_gpu.c

985

idle = gpu_read(gpu, VIVS_HI_IDLE_STATE);

drivers/gpu/drm/etnaviv/etnaviv_iommu_v2.c

172

if (gpu_read(gpu, VIVS_MMUv2_CONTROL) & VIVS_MMUv2_CONTROL_ENABLE)

drivers/gpu/drm/etnaviv/etnaviv_iommu_v2.c

196

if (gpu_read(gpu, VIVS_MMUv2_SEC_CONTROL) & VIVS_MMUv2_SEC_CONTROL_ENABLE)

drivers/gpu/drm/etnaviv/etnaviv_perfmon.c

110

return gpu_read(gpu, reg);

drivers/gpu/drm/etnaviv/etnaviv_perfmon.c

124

return gpu_read(gpu, reg);

drivers/gpu/drm/etnaviv/etnaviv_perfmon.c

46

return gpu_read(gpu, domain->profile_read);

drivers/gpu/drm/etnaviv/etnaviv_perfmon.c

61

u32 clock = gpu_read(gpu, VIVS_HI_CLOCK_CONTROL);

drivers/gpu/drm/etnaviv/etnaviv_perfmon.c

82

u32 clock = gpu_read(gpu, VIVS_HI_CLOCK_CONTROL);

drivers/gpu/drm/etnaviv/etnaviv_perfmon.c

90

value += gpu_read(gpu, signal->data);

drivers/gpu/drm/etnaviv/etnaviv_sched.c

54

dma_addr = gpu_read(gpu, VIVS_FE_DMA_ADDRESS);

drivers/gpu/drm/etnaviv/etnaviv_sched.c

62

primid = gpu_read(gpu, VIVS_MC_PROFILE_FE_READ);

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

277

gpu_read(gpu, REG_AXXX_CP_SCRATCH_REG0 + i));

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

285

gpu_read(gpu, REG_A2XX_RBBM_SOFT_RESET);

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

309

if (spin_until(!(gpu_read(gpu, REG_A2XX_RBBM_STATUS) &

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

324

mstatus = gpu_read(gpu, REG_A2XX_MASTER_INT_SIGNAL);

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

327

status = gpu_read(gpu, REG_A2XX_MH_INTERRUPT_STATUS);

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

331

gpu_read(gpu, REG_A2XX_MH_MMU_PAGE_FAULT));

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

337

status = gpu_read(gpu, REG_AXXX_CP_INT_STATUS);

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

347

status = gpu_read(gpu, REG_A2XX_RBBM_INT_STATUS);

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

454

gpu_read(gpu, REG_A2XX_RBBM_STATUS));

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

467

state->rbbm_status = gpu_read(gpu, REG_A2XX_RBBM_STATUS);

drivers/gpu/drm/msm/adreno/a2xx_gpu.c

488

ring->memptrs->rptr = gpu_read(gpu, REG_AXXX_CP_RB_RPTR);

drivers/gpu/drm/msm/adreno/a3xx_gpu.c

374

gpu_read(gpu, REG_AXXX_CP_SCRATCH_REG0 + i));

drivers/gpu/drm/msm/adreno/a3xx_gpu.c

382

gpu_read(gpu, REG_A3XX_RBBM_SW_RESET_CMD);

drivers/gpu/drm/msm/adreno/a3xx_gpu.c

408

if (spin_until(!(gpu_read(gpu, REG_A3XX_RBBM_STATUS) &

drivers/gpu/drm/msm/adreno/a3xx_gpu.c

423

status = gpu_read(gpu, REG_A3XX_RBBM_INT_0_STATUS);

drivers/gpu/drm/msm/adreno/a3xx_gpu.c

477

gpu_read(gpu, REG_A3XX_RBBM_STATUS));

drivers/gpu/drm/msm/adreno/a3xx_gpu.c

490

state->rbbm_status = gpu_read(gpu, REG_A3XX_RBBM_STATUS);

drivers/gpu/drm/msm/adreno/a3xx_gpu.c

507

ring->memptrs->rptr = gpu_read(gpu, REG_AXXX_CP_RB_RPTR);

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

277

val = gpu_read(gpu, REG_A4XX_RBBM_CLOCK_DELAY_HLSQ);

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

358

gpu_read(gpu, REG_AXXX_CP_SCRATCH_REG0 + i));

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

366

gpu_read(gpu, REG_A4XX_RBBM_SW_RESET_CMD);

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

392

if (spin_until(!(gpu_read(gpu, REG_A4XX_RBBM_STATUS) &

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

406

status = gpu_read(gpu, REG_A4XX_RBBM_INT_0_STATUS);

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

410

uint32_t reg = gpu_read(gpu, REG_A4XX_CP_PROTECT_STATUS);

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

560

state->rbbm_status = gpu_read(gpu, REG_A4XX_RBBM_STATUS);

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

568

gpu_read(gpu, REG_A4XX_RBBM_STATUS));

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

586

reg = gpu_read(gpu, REG_A4XX_RBBM_POWER_STATUS);

drivers/gpu/drm/msm/adreno/a4xx_gpu.c

626

ring->memptrs->rptr = gpu_read(gpu, REG_A4XX_CP_RB_RPTR);

drivers/gpu/drm/msm/adreno/a5xx_debugfs.c

23

gpu_read(gpu, REG_A5XX_CP_PFP_STAT_DATA));

drivers/gpu/drm/msm/adreno/a5xx_debugfs.c

36

gpu_read(gpu, REG_A5XX_CP_ME_STAT_DATA));

drivers/gpu/drm/msm/adreno/a5xx_debugfs.c

49

gpu_read(gpu, REG_A5XX_CP_MEQ_DBG_DATA));

drivers/gpu/drm/msm/adreno/a5xx_debugfs.c

64

val[j] = gpu_read(gpu, REG_A5XX_CP_ROQ_DBG_DATA);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1023

gpu_read(gpu, REG_A5XX_CP_SCRATCH_REG(i)));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1030

gpu_read(gpu, REG_A5XX_RBBM_SW_RESET_CMD);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1070

if (gpu_read(gpu, REG_A5XX_RBBM_STATUS) & ~A5XX_RBBM_STATUS_HI_BUSY)

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1077

return !(gpu_read(gpu, REG_A5XX_RBBM_INT_0_STATUS) &

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1098

gpu_read(gpu, REG_A5XX_RBBM_STATUS),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1099

gpu_read(gpu, REG_A5XX_RBBM_INT_0_STATUS),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1100

gpu_read(gpu, REG_A5XX_CP_RB_RPTR),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1101

gpu_read(gpu, REG_A5XX_CP_RB_WPTR));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1114

gpu_read(gpu, REG_A5XX_CP_SCRATCH_REG(4)),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1115

gpu_read(gpu, REG_A5XX_CP_SCRATCH_REG(5)),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1116

gpu_read(gpu, REG_A5XX_CP_SCRATCH_REG(6)),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1117

gpu_read(gpu, REG_A5XX_CP_SCRATCH_REG(7)),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1128

u32 status = gpu_read(gpu, REG_A5XX_CP_INTERRUPT_STATUS);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1140

gpu_read(gpu, REG_A5XX_CP_PFP_STAT_DATA);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1141

val = gpu_read(gpu, REG_A5XX_CP_PFP_STAT_DATA);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1149

gpu_read(gpu, REG_A5XX_CP_HW_FAULT));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1155

u32 val = gpu_read(gpu, REG_A5XX_CP_PROTECT_STATUS);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1164

u32 status = gpu_read(gpu, REG_A5XX_CP_AHB_FAULT);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1180

u32 val = gpu_read(gpu, REG_A5XX_RBBM_AHB_ERROR_STATUS);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1201

gpu_read(gpu, REG_A5XX_RBBM_AHB_ME_SPLIT_STATUS));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1205

gpu_read(gpu, REG_A5XX_RBBM_AHB_PFP_SPLIT_STATUS));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1209

gpu_read(gpu, REG_A5XX_RBBM_AHB_ETS_SPLIT_STATUS));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1220

uint64_t addr = (uint64_t) gpu_read(gpu, REG_A5XX_UCHE_TRAP_LOG_HI);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1222

addr |= gpu_read(gpu, REG_A5XX_UCHE_TRAP_LOG_LO);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1244

if (gpu_read(gpu, REG_A5XX_RBBM_STATUS3) & BIT(24))

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1249

gpu_read(gpu, REG_A5XX_RBBM_STATUS),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1250

gpu_read(gpu, REG_A5XX_CP_RB_RPTR),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1251

gpu_read(gpu, REG_A5XX_CP_RB_WPTR),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1253

gpu_read(gpu, REG_A5XX_CP_IB1_BUFSZ),

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1255

gpu_read(gpu, REG_A5XX_CP_IB2_BUFSZ));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1274

u32 status = gpu_read(gpu, REG_A5XX_RBBM_INT_0_STATUS);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1349

gpu_read(gpu, REG_A5XX_RBBM_STATUS));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1384

gpu_read(gpu, REG_A5XX_GPMU_RBCCU_PWR_CLK_STATUS));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1413

spin_until((gpu_read(gpu, REG_A5XX_VBIF_XIN_HALT_CTRL1) &

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1574

bool stalled = !!(gpu_read(gpu, REG_A5XX_RBBM_STATUS3) & BIT(24));

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1585

a5xx_state->base.rbbm_status = gpu_read(gpu, REG_A5XX_RBBM_STATUS);

drivers/gpu/drm/msm/adreno/a5xx_gpu.c

1690

return ring->memptrs->rptr = gpu_read(gpu, REG_A5XX_CP_RB_RPTR);

drivers/gpu/drm/msm/adreno/a5xx_gpu.h

146

if ((gpu_read(gpu, reg) & mask) == value)

drivers/gpu/drm/msm/adreno/a5xx_power.c

267

u32 val = gpu_read(gpu, REG_A5XX_GPMU_GENERAL_1);

drivers/gpu/drm/msm/adreno/a5xx_preempt.c

194

status = gpu_read(gpu, REG_A5XX_CP_CONTEXT_SWITCH_CNTL);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

120

if (gpu_read(gpu, REG_A6XX_RBBM_STATUS) &

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

124

return !(gpu_read(gpu, REG_A6XX_RBBM_INT_0_STATUS) &

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1266

gpu_read(gpu, REG_A6XX_GBIF_HALT);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1269

gpu_read(gpu, REG_A6XX_RBBM_GPR0_CNTL);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1272

gpu_read(gpu, REG_A6XX_GBIF_HALT);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1275

gpu_read(gpu, REG_A6XX_RBBM_GBIF_HALT);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

137

gpu_read(gpu, REG_A6XX_RBBM_STATUS),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

138

gpu_read(gpu, REG_A6XX_RBBM_INT_0_STATUS),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

139

gpu_read(gpu, REG_A6XX_CP_RB_RPTR),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

140

gpu_read(gpu, REG_A6XX_CP_RB_WPTR));

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1625

gpu_read(gpu, REG_A6XX_RBBM_STATUS));

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1725

val = gpu_read(gpu, REG_A6XX_UCHE_CLIENT_PF);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1827

gpu_read(gpu, REG_A6XX_CP_SCRATCH(4)),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1828

gpu_read(gpu, REG_A6XX_CP_SCRATCH(5)),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1829

gpu_read(gpu, REG_A6XX_CP_SCRATCH(6)),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1830

gpu_read(gpu, REG_A6XX_CP_SCRATCH(7)),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1841

u32 status = gpu_read(gpu, REG_A6XX_CP_INTERRUPT_STATUS);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1847

val = gpu_read(gpu, REG_A6XX_CP_SQE_STAT_DATA);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1859

gpu_read(gpu, REG_A6XX_CP_HW_FAULT));

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1862

u32 val = gpu_read(gpu, REG_A6XX_CP_PROTECT_STATUS);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1891

if (gpu_read(gpu, REG_A6XX_RBBM_STATUS3) & A6XX_RBBM_STATUS3_SMMU_STALLED_ON_FAULT)

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1897

gpu_read(gpu, REG_A6XX_RBBM_STATUS),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1898

gpu_read(gpu, REG_A6XX_CP_RB_RPTR),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1899

gpu_read(gpu, REG_A6XX_CP_RB_WPTR),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1901

gpu_read(gpu, REG_A6XX_CP_IB1_REM_SIZE),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1903

gpu_read(gpu, REG_A6XX_CP_IB2_REM_SIZE));

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1918

status = gpu_read(gpu, REG_A7XX_RBBM_SW_FUSE_INT_STATUS);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

1978

u32 status = gpu_read(gpu, REG_A6XX_RBBM_INT_0_STATUS);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2217

spin_until((gpu_read(gpu, REG_A6XX_RBBM_VBIF_GX_RESET_STATUS) &

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2221

spin_until((gpu_read(gpu, REG_A6XX_VBIF_XIN_HALT_CTRL1) &

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2231

spin_until(gpu_read(gpu, REG_A6XX_RBBM_GBIF_HALT_ACK) & 1);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2236

spin_until((gpu_read(gpu, REG_A6XX_GBIF_HALT_ACK) &

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2241

spin_until((gpu_read(gpu, REG_A6XX_GBIF_HALT_ACK) &

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2256

gpu_read(gpu, REG_A6XX_RBBM_SW_RESET_CMD);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2544

return ring->memptrs->rptr = gpu_read(gpu, REG_A6XX_CP_RB_RPTR);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2564

.ib1_rem = gpu_read(gpu, REG_A6XX_CP_IB1_REM_SIZE),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2565

.ib2_rem = gpu_read(gpu, REG_A6XX_CP_IB2_REM_SIZE),

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2581

cp_state.ib1_rem += gpu_read(gpu, REG_A6XX_CP_ROQ_AVAIL_IB1) >> 16;

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

2582

cp_state.ib2_rem += gpu_read(gpu, REG_A6XX_CP_ROQ_AVAIL_IB2) >> 16;

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

687

val = gpu_read(gpu, REG_A6XX_RBBM_CLOCK_CNTL);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

894

*dest++ = gpu_read(gpu, reglist->regs[i]);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

903

*dest++ = gpu_read(gpu, reglist->regs[i]);

drivers/gpu/drm/msm/adreno/a6xx_gpu.c

931

*dest++ = gpu_read(gpu, dyn_pwrup_reglist->regs[i].offset);

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

1149

obj->data[index++] = gpu_read(gpu,

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

1174

obj->data[index++] = gpu_read(gpu, regs[i] + j);

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

1446

return gpu_read(gpu, REG_A6XX_CP_ROQ_THRESHOLDS_2) >> 14;

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

1458

return 4 * (gpu_read(gpu, REG_A6XX_CP_SQE_UCODE_DBG_DATA) >> 20);

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

1484

obj->data[i] = gpu_read(gpu, indexed->data);

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

1506

val = gpu_read(gpu, REG_A6XX_CP_CHICKEN_DBG);

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

1519

mempool_size = gpu_read(gpu, REG_A6XX_CP_MEM_POOL_SIZE);

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

1622

stalled = !!(gpu_read(gpu, REG_A6XX_RBBM_STATUS3) &

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

195

data[0] = gpu_read(gpu, REG_A6XX_DBGC_CFG_DBGBUS_TRACE_BUF2);

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

196

data[1] = gpu_read(gpu, REG_A6XX_DBGC_CFG_DBGBUS_TRACE_BUF1);

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

245

data[i] = gpu_read(gpu, REG_A6XX_VBIF_TEST_BUS_OUT);

drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c

275

clk = gpu_read(gpu, REG_A6XX_VBIF_CLKON);

drivers/gpu/drm/msm/adreno/a6xx_preempt.c

174

status = gpu_read(gpu, REG_A6XX_CP_CONTEXT_SWITCH_CNTL);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1008

gpu_read(gpu, REG_A8XX_RBBM_STATUS), gpu_read(gpu, REG_A8XX_RBBM_GFX_STATUS));

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1014

gpu_read(gpu, REG_A8XX_RBBM_GFX_BR_STATUS),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1015

gpu_read(gpu, REG_A6XX_CP_RB_RPTR),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1016

gpu_read(gpu, REG_A6XX_CP_RB_WPTR),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1029

gpu_read(gpu, REG_A8XX_RBBM_GFX_BV_STATUS),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1030

gpu_read(gpu, REG_A8XX_CP_RB_RPTR_BV),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1031

gpu_read(gpu, REG_A6XX_CP_RB_WPTR),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1052

status = gpu_read(gpu, REG_A8XX_RBBM_SW_FUSE_INT_STATUS);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1072

u32 status = gpu_read(gpu, REG_A8XX_RBBM_INT_0_STATUS);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1085

rl0 = gpu_read(gpu, REG_A8XX_CP_RL_ERROR_DETAILS_0);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1086

rl1 = gpu_read(gpu, REG_A8XX_CP_RL_ERROR_DETAILS_1);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1160

spin_until(gpu_read(gpu, REG_A8XX_RBBM_GBIF_HALT_ACK) & 1);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1165

spin_until((gpu_read(gpu, REG_A6XX_GBIF_HALT_ACK) &

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

1170

spin_until((gpu_read(gpu, REG_A6XX_GBIF_HALT_ACK) &

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

130

if (gpu_read(gpu, REG_A8XX_RBBM_STATUS) &

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

134

return !(gpu_read(gpu, REG_A8XX_RBBM_INT_0_STATUS) &

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

148

gpu_read(gpu, REG_A8XX_RBBM_STATUS),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

149

gpu_read(gpu, REG_A8XX_RBBM_INT_0_STATUS),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

150

gpu_read(gpu, REG_A6XX_CP_RB_RPTR),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

151

gpu_read(gpu, REG_A6XX_CP_RB_WPTR));

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

524

gpu_read(gpu, REG_A6XX_GBIF_HALT);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

527

gpu_read(gpu, REG_A8XX_RBBM_GBIF_HALT);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

732

DRM_DEV_INFO(&gpu->pdev->dev, "status: %08x\n", gpu_read(gpu, REG_A8XX_RBBM_STATUS));

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

79

val = gpu_read(gpu, offset);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

815

val = gpu_read(gpu, REG_A8XX_UCHE_CLIENT_PF);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

872

gpu_read(gpu, REG_A8XX_CP_SCRATCH_GLOBAL(0)),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

873

gpu_read(gpu, REG_A8XX_CP_SCRATCH_GLOBAL(1)),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

874

gpu_read(gpu, REG_A8XX_CP_SCRATCH_GLOBAL(2)),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

875

gpu_read(gpu, REG_A8XX_CP_SCRATCH_GLOBAL(3)),

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

886

u32 status = gpu_read(gpu, REG_A8XX_CP_INTERRUPT_STATUS_GLOBAL);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

956

return gpu_read(gpu, REG_A8XX_CP_SQE_UCODE_DBG_DATA_PIPE);

drivers/gpu/drm/msm/adreno/a8xx_gpu.c

995

if (gpu_read(gpu, REG_A8XX_RBBM_MISC_STATUS) & A8XX_RBBM_MISC_STATUS_SMMU_STALLED_ON_FAULT)

drivers/gpu/drm/msm/adreno/adreno_gpu.c

1066

uint32_t val = gpu_read(gpu, addr);

drivers/gpu/drm/msm/adreno/adreno_gpu.c

807

state->registers[pos++] = gpu_read(gpu, addr);

drivers/gpu/drm/msm/msm_gpu.c

687

current_cntrs[i] = gpu_read(gpu, gpu->perfcntrs[i].sample_reg);

drivers/gpu/drm/panfrost/panfrost_dump.c

97

dumpreg->value = gpu_read(pfdev, reg);

drivers/gpu/drm/panfrost/panfrost_gpu.c

148

quirks = gpu_read(pfdev, GPU_TILER_CONFIG);

drivers/gpu/drm/panfrost/panfrost_gpu.c

257

pfdev->features.l2_features = gpu_read(pfdev, GPU_L2_FEATURES);

drivers/gpu/drm/panfrost/panfrost_gpu.c

258

pfdev->features.core_features = gpu_read(pfdev, GPU_CORE_FEATURES);

drivers/gpu/drm/panfrost/panfrost_gpu.c

259

pfdev->features.tiler_features = gpu_read(pfdev, GPU_TILER_FEATURES);

drivers/gpu/drm/panfrost/panfrost_gpu.c

260

pfdev->features.mem_features = gpu_read(pfdev, GPU_MEM_FEATURES);

drivers/gpu/drm/panfrost/panfrost_gpu.c

261

pfdev->features.mmu_features = gpu_read(pfdev, GPU_MMU_FEATURES);

drivers/gpu/drm/panfrost/panfrost_gpu.c

262

pfdev->features.thread_features = gpu_read(pfdev, GPU_THREAD_FEATURES);

drivers/gpu/drm/panfrost/panfrost_gpu.c

263

pfdev->features.max_threads = gpu_read(pfdev, GPU_THREAD_MAX_THREADS);

drivers/gpu/drm/panfrost/panfrost_gpu.c

264

pfdev->features.thread_max_workgroup_sz = gpu_read(pfdev, GPU_THREAD_MAX_WORKGROUP_SIZE);

drivers/gpu/drm/panfrost/panfrost_gpu.c

265

pfdev->features.thread_max_barrier_sz = gpu_read(pfdev, GPU_THREAD_MAX_BARRIER_SIZE);

drivers/gpu/drm/panfrost/panfrost_gpu.c

268

pfdev->features.coherency_features = gpu_read(pfdev, GPU_COHERENCY_FEATURES);

drivers/gpu/drm/panfrost/panfrost_gpu.c

287

pfdev->features.afbc_features = gpu_read(pfdev, GPU_AFBC_FEATURES);

drivers/gpu/drm/panfrost/panfrost_gpu.c

289

pfdev->features.texture_features[i] = gpu_read(pfdev, GPU_TEXTURE_FEATURES(i));

drivers/gpu/drm/panfrost/panfrost_gpu.c

291

pfdev->features.as_present = gpu_read(pfdev, GPU_AS_PRESENT);

drivers/gpu/drm/panfrost/panfrost_gpu.c

293

pfdev->features.js_present = gpu_read(pfdev, GPU_JS_PRESENT);

drivers/gpu/drm/panfrost/panfrost_gpu.c

296

pfdev->features.js_features[i] = gpu_read(pfdev, GPU_JS_FEATURES(i));

drivers/gpu/drm/panfrost/panfrost_gpu.c

298

pfdev->features.shader_present = gpu_read(pfdev, GPU_SHADER_PRESENT_LO);

drivers/gpu/drm/panfrost/panfrost_gpu.c

299

pfdev->features.shader_present |= (u64)gpu_read(pfdev, GPU_SHADER_PRESENT_HI) << 32;

drivers/gpu/drm/panfrost/panfrost_gpu.c

301

pfdev->features.tiler_present = gpu_read(pfdev, GPU_TILER_PRESENT_LO);

drivers/gpu/drm/panfrost/panfrost_gpu.c

302

pfdev->features.tiler_present |= (u64)gpu_read(pfdev, GPU_TILER_PRESENT_HI) << 32;

drivers/gpu/drm/panfrost/panfrost_gpu.c

304

pfdev->features.l2_present = gpu_read(pfdev, GPU_L2_PRESENT_LO);

drivers/gpu/drm/panfrost/panfrost_gpu.c

305

pfdev->features.l2_present |= (u64)gpu_read(pfdev, GPU_L2_PRESENT_HI) << 32;

drivers/gpu/drm/panfrost/panfrost_gpu.c

308

pfdev->features.stack_present = gpu_read(pfdev, GPU_STACK_PRESENT_LO);

drivers/gpu/drm/panfrost/panfrost_gpu.c

309

pfdev->features.stack_present |= (u64)gpu_read(pfdev, GPU_STACK_PRESENT_HI) << 32;

drivers/gpu/drm/panfrost/panfrost_gpu.c

311

pfdev->features.thread_tls_alloc = gpu_read(pfdev, GPU_THREAD_TLS_ALLOC);

drivers/gpu/drm/panfrost/panfrost_gpu.c

313

gpu_id = gpu_read(pfdev, GPU_ID);

drivers/gpu/drm/panfrost/panfrost_gpu.c

32

fault_status = gpu_read(pfdev, GPU_FAULT_STATUS);

drivers/gpu/drm/panfrost/panfrost_gpu.c

33

state = gpu_read(pfdev, GPU_INT_STAT);

drivers/gpu/drm/panfrost/panfrost_gpu.c

38

u64 address = (u64) gpu_read(pfdev, GPU_FAULT_ADDRESS_HI) << 32;

drivers/gpu/drm/panfrost/panfrost_gpu.c

39

address |= gpu_read(pfdev, GPU_FAULT_ADDRESS_LO);

drivers/gpu/drm/panfrost/panfrost_gpu.c

410

hi = gpu_read(pfdev, GPU_CYCLE_COUNT_HI);

drivers/gpu/drm/panfrost/panfrost_gpu.c

411

lo = gpu_read(pfdev, GPU_CYCLE_COUNT_LO);

drivers/gpu/drm/panfrost/panfrost_gpu.c

412

} while (hi != gpu_read(pfdev, GPU_CYCLE_COUNT_HI));

drivers/gpu/drm/panfrost/panfrost_gpu.c

422

hi = gpu_read(pfdev, GPU_TIMESTAMP_HI);

drivers/gpu/drm/panfrost/panfrost_gpu.c

423

lo = gpu_read(pfdev, GPU_TIMESTAMP_LO);

drivers/gpu/drm/panfrost/panfrost_gpu.c

424

} while (hi != gpu_read(pfdev, GPU_TIMESTAMP_HI));

drivers/gpu/drm/panfrost/panfrost_gpu.c

563

flush_id = gpu_read(pfdev, GPU_LATEST_FLUSH_ID);

drivers/gpu/drm/panthor/panthor_device.c

45

if ((gpu_read(ptdev, GPU_COHERENCY_FEATURES) &

drivers/gpu/drm/panthor/panthor_device.h

415

if (!gpu_read(ptdev, __reg_prefix ## _INT_STAT)) \

drivers/gpu/drm/panthor/panthor_device.h

429

u32 status = gpu_read(ptdev, __reg_prefix ## _INT_RAWSTAT) & pirq->mask; \

drivers/gpu/drm/panthor/panthor_device.h

500

return (gpu_read(ptdev, reg) | ((u64)gpu_read(ptdev, reg + 4) << 32));

drivers/gpu/drm/panthor/panthor_device.h

513

hi1 = gpu_read(ptdev, reg + 4);

drivers/gpu/drm/panthor/panthor_device.h

514

lo = gpu_read(ptdev, reg);

drivers/gpu/drm/panthor/panthor_device.h

515

hi2 = gpu_read(ptdev, reg + 4);

drivers/gpu/drm/panthor/panthor_device.h

521

read_poll_timeout(gpu_read, val, cond, delay_us, timeout_us, false, \

drivers/gpu/drm/panthor/panthor_device.h

526

read_poll_timeout_atomic(gpu_read, val, cond, delay_us, timeout_us, \

drivers/gpu/drm/panthor/panthor_fw.c

1090

!(gpu_read(ptdev, JOB_INT_STAT) & JOB_INT_GLOBAL_IF))

drivers/gpu/drm/panthor/panthor_fw.c

1101

u32 status = gpu_read(ptdev, MCU_STATUS);

drivers/gpu/drm/panthor/panthor_fw.c

1126

halted = gpu_read(ptdev, MCU_STATUS) == MCU_STATUS_HALT;

drivers/gpu/drm/panthor/panthor_gpu.c

315

!(gpu_read(ptdev, GPU_INT_RAWSTAT) & GPU_IRQ_CLEAN_CACHES_COMPLETED))

drivers/gpu/drm/panthor/panthor_gpu.c

355

!(gpu_read(ptdev, GPU_INT_RAWSTAT) & GPU_IRQ_RESET_COMPLETED))

drivers/gpu/drm/panthor/panthor_gpu.c

74

l2_config = gpu_read(ptdev, GPU_L2_CONFIG);

drivers/gpu/drm/panthor/panthor_gpu.c

84

u32 fault_status = gpu_read(ptdev, GPU_FAULT_STATUS);

drivers/gpu/drm/panthor/panthor_hw.c

135

ptdev->gpu_info.csf_id = gpu_read(ptdev, GPU_CSF_ID);

drivers/gpu/drm/panthor/panthor_hw.c

136

ptdev->gpu_info.gpu_rev = gpu_read(ptdev, GPU_REVID);

drivers/gpu/drm/panthor/panthor_hw.c

137

ptdev->gpu_info.core_features = gpu_read(ptdev, GPU_CORE_FEATURES);

drivers/gpu/drm/panthor/panthor_hw.c

138

ptdev->gpu_info.l2_features = gpu_read(ptdev, GPU_L2_FEATURES);

drivers/gpu/drm/panthor/panthor_hw.c

139

ptdev->gpu_info.tiler_features = gpu_read(ptdev, GPU_TILER_FEATURES);

drivers/gpu/drm/panthor/panthor_hw.c

140

ptdev->gpu_info.mem_features = gpu_read(ptdev, GPU_MEM_FEATURES);

drivers/gpu/drm/panthor/panthor_hw.c

141

ptdev->gpu_info.mmu_features = gpu_read(ptdev, GPU_MMU_FEATURES);

drivers/gpu/drm/panthor/panthor_hw.c

142

ptdev->gpu_info.thread_features = gpu_read(ptdev, GPU_THREAD_FEATURES);

drivers/gpu/drm/panthor/panthor_hw.c

143

ptdev->gpu_info.max_threads = gpu_read(ptdev, GPU_THREAD_MAX_THREADS);

drivers/gpu/drm/panthor/panthor_hw.c

144

ptdev->gpu_info.thread_max_workgroup_size = gpu_read(ptdev, GPU_THREAD_MAX_WORKGROUP_SIZE);

drivers/gpu/drm/panthor/panthor_hw.c

145

ptdev->gpu_info.thread_max_barrier_size = gpu_read(ptdev, GPU_THREAD_MAX_BARRIER_SIZE);

drivers/gpu/drm/panthor/panthor_hw.c

146

ptdev->gpu_info.coherency_features = gpu_read(ptdev, GPU_COHERENCY_FEATURES);

drivers/gpu/drm/panthor/panthor_hw.c

148

ptdev->gpu_info.texture_features[i] = gpu_read(ptdev, GPU_TEXTURE_FEATURES(i));

drivers/gpu/drm/panthor/panthor_hw.c

150

ptdev->gpu_info.as_present = gpu_read(ptdev, GPU_AS_PRESENT);

drivers/gpu/drm/panthor/panthor_hw.c

228

ptdev->gpu_info.gpu_id = gpu_read(ptdev, GPU_ID);

drivers/gpu/drm/panthor/panthor_mmu.c

1706

fault_status = gpu_read(ptdev, AS_FAULTSTATUS(as));

drivers/gpu/drm/panthor/panthor_pwr.c

84

return gpu_read(ptdev, PWR_INT_RAWSTAT) & PWR_IRQ_RESET_COMPLETED;