Lines Matching refs:Ccsr
2414 CsrMatrix *Acsr, *Bcsr, *Ccsr; in MatProductNumeric_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE() local
2435 Ccsr = (CsrMatrix *)Cmat->mat; in MatProductNumeric_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2436 PetscCheck(Ccsr, PetscObjectComm((PetscObject)C), PETSC_ERR_GPU, "Missing C CSR struct"); in MatProductNumeric_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2486 Ccsr = (CsrMatrix *)Cmat->mat; in MatProductNumeric_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2489 PetscCheck(Ccsr, PetscObjectComm((PetscObject)C), PETSC_ERR_GPU, "Missing C CSR struct"); in MatProductNumeric_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2502 …a().get(), Bcsr->column_indices->data().get(), Cmat->descr, Ccsr->values->data().get(), Ccsr->row_… in MatProductNumeric_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2503 Ccsr->column_indices->data().get())); in MatProductNumeric_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2529 CsrMatrix *Acsr, *Bcsr, *Ccsr; in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE() local
2616 Ccsr = new CsrMatrix; in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2635 Ccusp->mat->mat = Ccsr; in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2636 Ccsr->num_rows = Ccusp->nrows; in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2637 Ccsr->num_cols = n; in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2638 Ccsr->row_offsets = new THRUSTINTARRAY32(Ccusp->nrows + 1); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2648 …if (!Ccsr->num_rows || !Ccsr->num_cols || !a->nz || !b->nz) { /* hipsparse raise errors in differe… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2649 thrust::fill(thrust::device, Ccsr->row_offsets->begin(), Ccsr->row_offsets->end(), 0); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2651 Ccsr->column_indices = new THRUSTINTARRAY32(c->nz); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2652 Ccsr->values = new THRUSTARRAY(c->nz); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2706 …PetscCallHIPSPARSE(hipsparseCreateCsr(&Cmat->matDescr, Ccsr->num_rows, Ccsr->num_cols, 0, Ccsr->ro… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2741 Ccsr->column_indices = new THRUSTINTARRAY32(c->nz); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2743 Ccsr->values = new THRUSTARRAY(c->nz); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2747 …hipsparseCsrSetPointers(Cmat->matDescr, Ccsr->row_offsets->data().get(), Ccsr->column_indices->dat… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2778 Ccsr->column_indices = new THRUSTINTARRAY32(c->nz); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2780 Ccsr->values = new THRUSTARRAY(c->nz); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2782 …hipsparseCsrSetPointers(Cmat->matDescr, Ccsr->row_offsets->data().get(), Ccsr->column_indices->dat… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2788 …w_offsets->data().get(), Bcsr->column_indices->data().get(), Cmat->descr, Ccsr->row_offsets->data(… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2790 Ccsr->column_indices = new THRUSTINTARRAY32(c->nz); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2792 Ccsr->values = new THRUSTARRAY(c->nz); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2800 …a().get(), Bcsr->column_indices->data().get(), Cmat->descr, Ccsr->values->data().get(), Ccsr->row_… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2801 Ccsr->column_indices->data().get())); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2812 THRUSTINTARRAY ii(Ccsr->row_offsets->size()); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2813 THRUSTINTARRAY jj(Ccsr->column_indices->size()); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2814 ii = *Ccsr->row_offsets; in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2815 jj = *Ccsr->column_indices; in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2817 …PetscCallHIP(hipMemcpy(d_i, ii.data().get(), Ccsr->row_offsets->size() * sizeof(PetscInt), hipMemc… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2818 …PetscCallHIP(hipMemcpy(c->j, jj.data().get(), Ccsr->column_indices->size() * sizeof(PetscInt), hip… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2822 …PetscCallHIP(hipMemcpy(d_i, Ccsr->row_offsets->data().get(), Ccsr->row_offsets->size() * sizeof(Pe… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2823 …PetscCallHIP(hipMemcpy(c->j, Ccsr->column_indices->data().get(), Ccsr->column_indices->size() * si… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2835 …PetscCall(PetscLogGpuToCpu((Ccsr->column_indices->size() + Ccsr->row_offsets->size()) * sizeof(Pet… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2848 Ccsr->num_entries = c->nz; in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
4097 CsrMatrix *Acsr, *Bcsr, *Ccsr; in MatSeqAIJHIPSPARSEMergeMats() local
4120 Ccsr = new CsrMatrix; in MatSeqAIJHIPSPARSEMergeMats()
4129 Ccusp->mat->mat = Ccsr; in MatSeqAIJHIPSPARSEMergeMats()
4130 Ccsr->num_rows = m; in MatSeqAIJHIPSPARSEMergeMats()
4131 Ccsr->num_cols = n; in MatSeqAIJHIPSPARSEMergeMats()
4151 Ccsr->row_offsets = new THRUSTINTARRAY32(m + 1); in MatSeqAIJHIPSPARSEMergeMats()
4152 Ccsr->column_indices = new THRUSTINTARRAY32(c->nz); in MatSeqAIJHIPSPARSEMergeMats()
4153 Ccsr->values = new THRUSTARRAY(c->nz); in MatSeqAIJHIPSPARSEMergeMats()
4154 Ccsr->num_entries = c->nz; in MatSeqAIJHIPSPARSEMergeMats()
4191 …hrust::make_zip_iterator(thrust::make_tuple(Ccoo->begin(), Ccsr->column_indices->begin(), Ccsr->va… in MatSeqAIJHIPSPARSEMergeMats()
4205 …PetscCallHIPSPARSE(hipsparseXcoo2csr(Ccusp->handle, Ccoo->data().get(), c->nz, m, Ccsr->row_offset… in MatSeqAIJHIPSPARSEMergeMats()
4211 …at->matDescr, Ccsr->num_rows, Ccsr->num_cols, Ccsr->num_entries, Ccsr->row_offsets->data().get(), … in MatSeqAIJHIPSPARSEMergeMats()
4273 THRUSTINTARRAY ii(Ccsr->row_offsets->size()); in MatSeqAIJHIPSPARSEMergeMats()
4274 THRUSTINTARRAY jj(Ccsr->column_indices->size()); in MatSeqAIJHIPSPARSEMergeMats()
4275 ii = *Ccsr->row_offsets; in MatSeqAIJHIPSPARSEMergeMats()
4276 jj = *Ccsr->column_indices; in MatSeqAIJHIPSPARSEMergeMats()
4277 …PetscCallHIP(hipMemcpy(c->i, ii.data().get(), Ccsr->row_offsets->size() * sizeof(PetscInt), hipMem… in MatSeqAIJHIPSPARSEMergeMats()
4278 …PetscCallHIP(hipMemcpy(c->j, jj.data().get(), Ccsr->column_indices->size() * sizeof(PetscInt), hip… in MatSeqAIJHIPSPARSEMergeMats()
4280 …PetscCallHIP(hipMemcpy(c->i, Ccsr->row_offsets->data().get(), Ccsr->row_offsets->size() * sizeof(P… in MatSeqAIJHIPSPARSEMergeMats()
4281 …PetscCallHIP(hipMemcpy(c->j, Ccsr->column_indices->data().get(), Ccsr->column_indices->size() * si… in MatSeqAIJHIPSPARSEMergeMats()
4283 …PetscCall(PetscLogGpuToCpu((Ccsr->column_indices->size() + Ccsr->row_offsets->size()) * sizeof(Pet… in MatSeqAIJHIPSPARSEMergeMats()
4315 Ccsr = (CsrMatrix *)Ccusp->mat->mat; in MatSeqAIJHIPSPARSEMergeMats()
4318 …Ccsr->num_entries == (PetscInt)Ccsr->values->size(), PETSC_COMM_SELF, PETSC_ERR_COR, "C nnz %" Pet… in MatSeqAIJHIPSPARSEMergeMats()
4319 …Ccsr->num_entries == Acsr->num_entries + Bcsr->num_entries, PETSC_COMM_SELF, PETSC_ERR_COR, "C nnz… in MatSeqAIJHIPSPARSEMergeMats()
4320 …= Ccsr->values->size(), PETSC_COMM_SELF, PETSC_ERR_COR, "permSize %" PetscInt_FMT " != %" PetscInt… in MatSeqAIJHIPSPARSEMergeMats()
4324 …rust::make_tuple(Acsr->values->begin(), thrust::make_permutation_iterator(Ccsr->values->begin(), C… in MatSeqAIJHIPSPARSEMergeMats()
4325 …thrust::make_tuple(Acsr->values->end(), thrust::make_permutation_iterator(Ccsr->values->begin(), p… in MatSeqAIJHIPSPARSEMergeMats()
4327 …rust::make_tuple(Bcsr->values->begin(), thrust::make_permutation_iterator(Ccsr->values->begin(), p… in MatSeqAIJHIPSPARSEMergeMats()
4328 …thrust::make_tuple(Bcsr->values->end(), thrust::make_permutation_iterator(Ccsr->values->begin(), C… in MatSeqAIJHIPSPARSEMergeMats()