Lines Matching refs:csrVal
231 PetscCallCUDA(cudaMalloc(&fs->csrVal, sizeof(*fs->csrVal) * Mnz)); in MatSeqAIJCUSPARSEBuildFactoredMatrix_LU()
244 …reateCsr(&fs->spMatDescr_L, m, m, Mnz, fs->csrRowPtr, fs->csrColIdx, fs->csrVal, indexType, indexT… in MatSeqAIJCUSPARSEBuildFactoredMatrix_LU()
250 …reateCsr(&fs->spMatDescr_U, m, m, Mnz, fs->csrRowPtr, fs->csrColIdx, fs->csrVal, indexType, indexT… in MatSeqAIJCUSPARSEBuildFactoredMatrix_LU()
285 PetscCallCUDA(cudaMemcpy(fs->csrVal, Ma, sizeof(*Ma) * Mnz, cudaMemcpyHostToDevice)); in MatSeqAIJCUSPARSEBuildFactoredMatrix_LU()
290 …if (fs->csrVal) PetscCallCUSPARSE(cusparseSpSV_updateMatrix(fs->handle, fs->spsvDescr_L, fs->csrVa… in MatSeqAIJCUSPARSEBuildFactoredMatrix_LU()
291 …if (fs->csrVal) PetscCallCUSPARSE(cusparseSpSV_updateMatrix(fs->handle, fs->spsvDescr_U, fs->csrVa… in MatSeqAIJCUSPARSEBuildFactoredMatrix_LU()
646 PetscCallCUDA(cudaMalloc(&fs->csrVal, sizeof(*fs->csrVal) * Mnz)); in MatSeqAIJCUSPARSEBuildFactoredMatrix_Cholesky()
660 …reateCsr(&fs->spMatDescr_U, m, m, Mnz, fs->csrRowPtr, fs->csrColIdx, fs->csrVal, indexType, indexT… in MatSeqAIJCUSPARSEBuildFactoredMatrix_Cholesky()
694 PetscCallCUDA(cudaMemcpy(fs->csrVal, Ma, sizeof(*Ma) * Mnz, cudaMemcpyHostToDevice)); in MatSeqAIJCUSPARSEBuildFactoredMatrix_Cholesky()
699 …if (fs->csrVal) PetscCallCUSPARSE(cusparseSpSV_updateMatrix(fs->handle, fs->spsvDescr_U, fs->csrVa… in MatSeqAIJCUSPARSEBuildFactoredMatrix_Cholesky()
700 …if (fs->csrVal) PetscCallCUSPARSE(cusparseSpSV_updateMatrix(fs->handle, fs->spsvDescr_Ut, fs->csrV… in MatSeqAIJCUSPARSEBuildFactoredMatrix_Cholesky()
1716 …PetscCallCUDA(cudaMemcpyAsync(fs->csrVal, Acsr->values->data().get(), sizeof(PetscScalar) * nz, cu… in MatILUFactorNumeric_SeqAIJCUSPARSE_ILU0()
1722 …fs->matDescr_M, fs->csrVal, fs->csrRowPtr32, fs->csrColIdx32, fs->ilu0Info_M, fs->policy_M, fs->fa… in MatILUFactorNumeric_SeqAIJCUSPARSE_ILU0()
1732 …if (fs->csrVal) PetscCallCUSPARSE(cusparseSpSV_updateMatrix(fs->handle, fs->spsvDescr_L, fs->csrVa… in MatILUFactorNumeric_SeqAIJCUSPARSE_ILU0()
1733 …if (fs->csrVal) PetscCallCUSPARSE(cusparseSpSV_updateMatrix(fs->handle, fs->spsvDescr_U, fs->csrVa… in MatILUFactorNumeric_SeqAIJCUSPARSE_ILU0()
1804 PetscCallCUDA(cudaMalloc((void **)&fs->csrVal, sizeof(*fs->csrVal) * nz)); in MatILUFactorSymbolic_SeqAIJCUSPARSE_ILU0()
1827 …teCsr(&fs->spMatDescr_L, m, m, nz, fs->csrRowPtr32, fs->csrColIdx32, fs->csrVal, CUSPARSE_INDEX_32… in MatILUFactorSymbolic_SeqAIJCUSPARSE_ILU0()
1833 …teCsr(&fs->spMatDescr_U, m, m, nz, fs->csrRowPtr32, fs->csrColIdx32, fs->csrVal, CUSPARSE_INDEX_32… in MatILUFactorSymbolic_SeqAIJCUSPARSE_ILU0()
1843 …fs->matDescr_M, fs->csrVal, fs->csrRowPtr32, fs->csrColIdx32, fs->ilu0Info_M, &fs->factBufferSize_… in MatILUFactorSymbolic_SeqAIJCUSPARSE_ILU0()
1882 …fs->matDescr_M, fs->csrVal, fs->csrRowPtr32, fs->csrColIdx32, fs->ilu0Info_M, fs->policy_M, fs->fa… in MatILUFactorSymbolic_SeqAIJCUSPARSE_ILU0()
1966 …PetscCallCUDA(cudaMemcpyAsync(fs->csrVal, Acsr->values->data().get(), sizeof(PetscScalar) * nz, cu… in MatICCFactorNumeric_SeqAIJCUSPARSE_ICC0()
1975 …if (m) PetscCallCUSPARSE(cusparseXcsric02(fs->handle, m, nz, fs->matDescr_M, fs->csrVal, fs->csrRo… in MatICCFactorNumeric_SeqAIJCUSPARSE_ICC0()
1985 …if (fs->csrVal) PetscCallCUSPARSE(cusparseSpSV_updateMatrix(fs->handle, fs->spsvDescr_L, fs->csrVa… in MatICCFactorNumeric_SeqAIJCUSPARSE_ICC0()
1986 …if (fs->csrVal) PetscCallCUSPARSE(cusparseSpSV_updateMatrix(fs->handle, fs->spsvDescr_Lt, fs->csrV… in MatICCFactorNumeric_SeqAIJCUSPARSE_ICC0()
2053 PetscCallCUDA(cudaMalloc((void **)&fs->csrVal, sizeof(PetscScalar) * nz)); in MatICCFactorSymbolic_SeqAIJCUSPARSE_ICC0()
2076 …teCsr(&fs->spMatDescr_L, m, m, nz, fs->csrRowPtr32, fs->csrColIdx32, fs->csrVal, CUSPARSE_INDEX_32… in MatICCFactorSymbolic_SeqAIJCUSPARSE_ICC0()
2084 …PARSE(cusparseXcsric02_bufferSize(fs->handle, m, nz, fs->matDescr_M, fs->csrVal, fs->csrRowPtr32, … in MatICCFactorSymbolic_SeqAIJCUSPARSE_ICC0()
2119 …if (m) PetscCallCUSPARSE(cusparseXcsric02_analysis(fs->handle, m, nz, fs->matDescr_M, fs->csrVal, … in MatICCFactorSymbolic_SeqAIJCUSPARSE_ICC0()
2332 else if (fs->csrVal) { in MatSeqAIJCUSPARSECopyFromGPU()
2334 … PetscCallCUDA(cudaMemcpy(a->a, fs->csrVal, a->nz * sizeof(PetscScalar), cudaMemcpyDeviceToHost)); in MatSeqAIJCUSPARSECopyFromGPU()
4295 PetscCallCUDA(cudaFree(fs->csrVal)); in MatSeqAIJCUSPARSETriFactors_Reset()