Lines Matching refs:batch_idx_write
41 (idxd->batch_idx_write * sizeof(struct idxd_completion)); in __submit()
65 if (++idxd->batch_idx_write > idxd->max_batches) in __submit()
66 idxd->batch_idx_write = 0; in __submit()
72 idxd->batch_idx_ring[idxd->batch_idx_write] = idxd->batch_start; in __submit()
73 _mm256_store_si256((void *)&idxd->batch_comp_ring[idxd->batch_idx_write], in __submit()
91 if ((idxd->batch_idx_read == 0 && idxd->batch_idx_write == idxd->max_batches) || in __idxd_write_desc()
92 idxd->batch_idx_write + 1 == idxd->batch_idx_read) in __idxd_write_desc()
171 uint16_t last_batch_write = idxd->batch_idx_write == 0 ? idxd->max_batches : in idxd_vchan_status()
172 idxd->batch_idx_write - 1; in idxd_vchan_status()
201 if (idxd->batch_idx_read == idxd->batch_idx_write) in batch_ok()
417 if (i == idxd->batch_idx_read && i == idxd->batch_idx_write) in idxd_dump()
421 else if (i == idxd->batch_idx_write) in idxd_dump()
479 if ((idxd->batch_idx_read == 0 && idxd->batch_idx_write == idxd->max_batches) || in idxd_burst_capacity()
480 idxd->batch_idx_write + 1 == idxd->batch_idx_read) in idxd_burst_capacity()
531 idxd->batch_idx_write = 0; in idxd_vchan_setup()