Lines Matching refs:cuSpMV

3659       if (!matstruct->cuSpMV[opA].initialized) { /* built on demand */  in MatMultAddKernel_SeqAIJCUSPARSE()
3660 …PetscCallCUSPARSE(cusparseCreateDnVec(&matstruct->cuSpMV[opA].vecXDescr, nx, xptr, cusparse_scalar… in MatMultAddKernel_SeqAIJCUSPARSE()
3661 …PetscCallCUSPARSE(cusparseCreateDnVec(&matstruct->cuSpMV[opA].vecYDescr, ny, dptr, cusparse_scalar… in MatMultAddKernel_SeqAIJCUSPARSE()
3663 …, matstruct->cuSpMV[opA].vecXDescr, beta, matstruct->cuSpMV[opA].vecYDescr, cusparse_scalartype, c… in MatMultAddKernel_SeqAIJCUSPARSE()
3664 …PetscCallCUDA(cudaMalloc(&matstruct->cuSpMV[opA].spmvBuffer, matstruct->cuSpMV[opA].spmvBufferSize… in MatMultAddKernel_SeqAIJCUSPARSE()
3667 …, matstruct->cuSpMV[opA].vecXDescr, beta, matstruct->cuSpMV[opA].vecYDescr, cusparse_scalartype, c… in MatMultAddKernel_SeqAIJCUSPARSE()
3669 matstruct->cuSpMV[opA].initialized = PETSC_TRUE; in MatMultAddKernel_SeqAIJCUSPARSE()
3672 PetscCallCUSPARSE(cusparseDnVecSetValues(matstruct->cuSpMV[opA].vecXDescr, xptr)); in MatMultAddKernel_SeqAIJCUSPARSE()
3673 PetscCallCUSPARSE(cusparseDnVecSetValues(matstruct->cuSpMV[opA].vecYDescr, dptr)); in MatMultAddKernel_SeqAIJCUSPARSE()
3676 …, matstruct->cuSpMV[opA].vecXDescr, beta, matstruct->cuSpMV[opA].vecYDescr, cusparse_scalartype, c… in MatMultAddKernel_SeqAIJCUSPARSE()
4254 if (mdata->cuSpMV[i].initialized) { in MatSeqAIJCUSPARSEMultStruct_Destroy()
4255 PetscCallCUDA(cudaFree(mdata->cuSpMV[i].spmvBuffer)); in MatSeqAIJCUSPARSEMultStruct_Destroy()
4256 PetscCallCUSPARSE(cusparseDestroyDnVec(mdata->cuSpMV[i].vecXDescr)); in MatSeqAIJCUSPARSEMultStruct_Destroy()
4257 PetscCallCUSPARSE(cusparseDestroyDnVec(mdata->cuSpMV[i].vecYDescr)); in MatSeqAIJCUSPARSEMultStruct_Destroy()