CLEAN
THEAD_CMO_OP(CLEAN, paddr, size, riscv_cbom_block_size);
regs->status = __riscv_v_vstate_or(regs->status, CLEAN);
ALT_CMO_OP(CLEAN, vaddr, size, riscv_cbom_block_size);
ALT_CMO_OP(CLEAN, addr, size, riscv_cbom_block_size);
if (atomic_read_acquire(&kvm->arch.apic_map_dirty) == CLEAN)
DIRTY, UPDATE_IN_PROGRESS) == CLEAN) {
UPDATE_IN_PROGRESS, CLEAN);
if (TREE_EMPTY(d, CLEAN))
clean_root = TREE_ROOT(d, CLEAN);
TREE_COUNT(d, CLEAN)--;
return TREE_COUNT(d, CLEAN) * d->pages_per_eblk +
if (TREE_COUNT(d, CLEAN) < LOW_FRAG_GC_THRESHOLD)
(background || (TREE_EMPTY(d, CLEAN) && TREE_EMPTY(d, DIRTY))))
if (background && TREE_COUNT(d, CLEAN) > CLEAN_BLOCK_THRESHOLD &&
__XFS_IS_OPSTATE(clean, CLEAN)