Lines Matching refs:PetscCallHIP
280 PetscCallHIP(hipHostMalloc((void **)&AALo, nzLower * sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
283 PetscCallHIP(hipHostMalloc((void **)&AiLo, (n + 1) * sizeof(PetscInt))); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
284 PetscCallHIP(hipHostMalloc((void **)&AjLo, nzLower * sizeof(PetscInt))); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
342 PetscCallHIP(hipMalloc(&loTriFactor->solveBuffer, loTriFactor->solveBufferSize)); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
348 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
354 PetscCallHIP(hipHostFree(AiLo)); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
355 PetscCallHIP(hipHostFree(AjLo)); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
358 …if (!loTriFactor->AA_h) PetscCallHIP(hipHostMalloc((void **)&loTriFactor->AA_h, nzLower * sizeof(P… in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
402 PetscCallHIP(hipHostMalloc((void **)&AAUp, nzUpper * sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
405 PetscCallHIP(hipHostMalloc((void **)&AiUp, (n + 1) * sizeof(PetscInt))); in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
406 PetscCallHIP(hipHostMalloc((void **)&AjUp, nzUpper * sizeof(PetscInt))); in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
458 PetscCallHIP(hipMalloc(&upTriFactor->solveBuffer, upTriFactor->solveBufferSize)); in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
464 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
470 PetscCallHIP(hipHostFree(AiUp)); in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
471 PetscCallHIP(hipHostFree(AjUp)); in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
474 …if (!upTriFactor->AA_h) PetscCallHIP(hipHostMalloc((void **)&upTriFactor->AA_h, nzUpper * sizeof(P… in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
556 PetscCallHIP(hipHostMalloc((void **)&AAUp, nzUpper * sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
557 PetscCallHIP(hipHostMalloc((void **)&AALo, nzUpper * sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
560 PetscCallHIP(hipHostMalloc((void **)&AiUp, (n + 1) * sizeof(PetscInt))); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
561 PetscCallHIP(hipHostMalloc((void **)&AjUp, nzUpper * sizeof(PetscInt))); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
622 PetscCallHIP(hipMalloc(&upTriFactor->solveBuffer, upTriFactor->solveBufferSize)); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
628 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
665 PetscCallHIP(hipMalloc(&loTriFactor->solveBuffer, loTriFactor->solveBufferSize)); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
671 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
678 PetscCallHIP(hipHostFree(AiUp)); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
679 PetscCallHIP(hipHostFree(AjUp)); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
708 PetscCallHIP(hipHostFree(AAUp)); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
709 PetscCallHIP(hipHostFree(AALo)); in MatSeqAIJHIPSPARSEBuildICCTriMatrices()
844 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSEAnalyzeTransposeForSolve()
852 PetscCallHIP(hipMalloc(&loTriFactorT->solveBuffer, loTriFactorT->solveBufferSize)); in MatSeqAIJHIPSPARSEAnalyzeTransposeForSolve()
858 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSEAnalyzeTransposeForSolve()
916 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSEAnalyzeTransposeForSolve()
924 PetscCallHIP(hipMalloc(&upTriFactorT->solveBuffer, upTriFactorT->solveBufferSize)); in MatSeqAIJHIPSPARSEAnalyzeTransposeForSolve()
930 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSEAnalyzeTransposeForSolve()
967 PetscCallHIP(hipMalloc((void **)&matstructT->alpha_one, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEFormExplicitTranspose()
968 PetscCallHIP(hipMalloc((void **)&matstructT->beta_zero, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEFormExplicitTranspose()
969 PetscCallHIP(hipMalloc((void **)&matstructT->beta_one, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEFormExplicitTranspose()
970 …PetscCallHIP(hipMemcpy(matstructT->alpha_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpy… in MatSeqAIJHIPSPARSEFormExplicitTranspose()
971 …PetscCallHIP(hipMemcpy(matstructT->beta_zero, &PETSC_HIPSPARSE_ZERO, sizeof(PetscScalar), hipMemcp… in MatSeqAIJHIPSPARSEFormExplicitTranspose()
972 …PetscCallHIP(hipMemcpy(matstructT->beta_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpyH… in MatSeqAIJHIPSPARSEFormExplicitTranspose()
1301 PetscCallHIP(hipMalloc((void **)&fs->spsvBuffer_Lt, fs->spsvBufferSize_Lt)); in MatSolveTranspose_SeqAIJHIPSPARSE_ILU0()
1302 PetscCallHIP(hipMalloc((void **)&fs->spsvBuffer_Ut, fs->spsvBufferSize_Ut)); in MatSolveTranspose_SeqAIJHIPSPARSE_ILU0()
1363 …PetscCallHIP(hipMemcpyAsync(fs->csrVal, Acsr->values->data().get(), sizeof(PetscScalar) * nz, hipM… in MatILUFactorNumeric_SeqAIJHIPSPARSE_ILU0()
1436 PetscCallHIP(hipMalloc((void **)&fs->csrRowPtr, sizeof(int) * (m + 1))); in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1437 PetscCallHIP(hipMalloc((void **)&fs->csrColIdx, sizeof(int) * nz)); in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1438 PetscCallHIP(hipMalloc((void **)&fs->csrVal, sizeof(PetscScalar) * nz)); in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1440 …PetscCallHIP(hipMemcpyAsync(fs->csrRowPtr, Ai, sizeof(int) * (m + 1), hipMemcpyDeviceToDevice, Pet… in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1441 …PetscCallHIP(hipMemcpyAsync(fs->csrColIdx, Aj, sizeof(int) * nz, hipMemcpyDeviceToDevice, PetscDef… in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1479 PetscCallHIP(hipMalloc((void **)&fs->X, sizeof(PetscScalar) * m)); in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1480 PetscCallHIP(hipMalloc((void **)&fs->Y, sizeof(PetscScalar) * m)); in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1495 …PetscCallHIP(hipMalloc((void **)&fs->factBuffer_M, PetscMax(fs->spsvBufferSize_L, (size_t)fs->fact… in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1497 PetscCallHIP(hipMalloc((void **)&fs->spsvBuffer_U, fs->spsvBufferSize_U)); in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1499 …PetscCallHIP(hipMalloc((void **)&fs->factBuffer_M, PetscMax(fs->spsvBufferSize_U, (size_t)fs->fact… in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1501 PetscCallHIP(hipMalloc((void **)&fs->spsvBuffer_L, fs->spsvBufferSize_L)); in MatILUFactorSymbolic_SeqAIJHIPSPARSE_ILU0()
1606 …PetscCallHIP(hipMemcpyAsync(fs->csrVal, Acsr->values->data().get(), sizeof(PetscScalar) * nz, hipM… in MatICCFactorNumeric_SeqAIJHIPSPARSE_ICC0()
1681 PetscCallHIP(hipMalloc((void **)&fs->csrRowPtr, sizeof(int) * (m + 1))); in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1682 PetscCallHIP(hipMalloc((void **)&fs->csrColIdx, sizeof(int) * nz)); in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1683 PetscCallHIP(hipMalloc((void **)&fs->csrVal, sizeof(PetscScalar) * nz)); in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1685 …PetscCallHIP(hipMemcpyAsync(fs->csrRowPtr, Ai, sizeof(int) * (m + 1), hipMemcpyDeviceToDevice, Pet… in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1686 …PetscCallHIP(hipMemcpyAsync(fs->csrColIdx, Aj, sizeof(int) * nz, hipMemcpyDeviceToDevice, PetscDef… in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1716 PetscCallHIP(hipMalloc((void **)&fs->X, sizeof(PetscScalar) * m)); in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1717 PetscCallHIP(hipMalloc((void **)&fs->Y, sizeof(PetscScalar) * m)); in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1732 …PetscCallHIP(hipMalloc((void **)&fs->factBuffer_M, PetscMax(fs->spsvBufferSize_L, (size_t)fs->fact… in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1734 PetscCallHIP(hipMalloc((void **)&fs->spsvBuffer_Lt, fs->spsvBufferSize_Lt)); in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1736 …PetscCallHIP(hipMalloc((void **)&fs->factBuffer_M, PetscMax(fs->spsvBufferSize_Lt, (size_t)fs->fac… in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1738 PetscCallHIP(hipMalloc((void **)&fs->spsvBuffer_L, fs->spsvBufferSize_L)); in MatICCFactorSymbolic_SeqAIJHIPSPARSE_ICC0()
1917 …PetscCallHIP(hipMemcpy(a->a, matrix->values->data().get(), a->nz * sizeof(PetscScalar), hipMemcpyD… in MatSeqAIJHIPSPARSECopyFromGPU()
1922 PetscCallHIP(hipMemcpy(a->a, fs->csrVal, a->nz * sizeof(PetscScalar), hipMemcpyDeviceToHost)); in MatSeqAIJHIPSPARSECopyFromGPU()
2029 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSECopyToGPU()
2066 PetscCallHIP(hipMalloc((void **)&matstruct->alpha_one, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSECopyToGPU()
2067 PetscCallHIP(hipMalloc((void **)&matstruct->beta_zero, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSECopyToGPU()
2068 PetscCallHIP(hipMalloc((void **)&matstruct->beta_one, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSECopyToGPU()
2069 …PetscCallHIP(hipMemcpy(matstruct->alpha_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpyH… in MatSeqAIJHIPSPARSECopyToGPU()
2070 …PetscCallHIP(hipMemcpy(matstruct->beta_zero, &PETSC_HIPSPARSE_ZERO, sizeof(PetscScalar), hipMemcpy… in MatSeqAIJHIPSPARSECopyToGPU()
2071 …PetscCallHIP(hipMemcpy(matstruct->beta_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpyHo… in MatSeqAIJHIPSPARSECopyToGPU()
2139 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSECopyToGPU()
2197 PetscCallHIP(hipFree(mmdata->Bt)); in MatProductCtxDestroy_MatMatHipsparse()
2204 if (mmdata->dBuffer4) PetscCallHIP(hipFree(mmdata->dBuffer4)); in MatProductCtxDestroy_MatMatHipsparse()
2205 if (mmdata->dBuffer5) PetscCallHIP(hipFree(mmdata->dBuffer5)); in MatProductCtxDestroy_MatMatHipsparse()
2207 if (mmdata->mmBuffer) PetscCallHIP(hipFree(mmdata->mmBuffer)); in MatProductCtxDestroy_MatMatHipsparse()
2208 if (mmdata->mmBuffer2) PetscCallHIP(hipFree(mmdata->mmBuffer2)); in MatProductCtxDestroy_MatMatHipsparse()
2313 PetscCallHIP(hipFree(mmdata->mmBuffer)); in MatProductNumeric_SeqAIJHIPSPARSE_SeqDENSEHIP()
2314 PetscCallHIP(hipMalloc(&mmdata->mmBuffer, mmBufferSize)); in MatProductNumeric_SeqAIJHIPSPARSE_SeqDENSEHIP()
2506 PetscCallHIP(WaitForHIP()); in MatProductNumeric_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2642 PetscCallHIP(hipMalloc((void **)&Cmat->alpha_one, sizeof(PetscScalar))); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2643 PetscCallHIP(hipMalloc((void **)&Cmat->beta_zero, sizeof(PetscScalar))); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2644 PetscCallHIP(hipMalloc((void **)&Cmat->beta_one, sizeof(PetscScalar))); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2645 …PetscCallHIP(hipMemcpy(Cmat->alpha_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpyHostTo… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2646 …PetscCallHIP(hipMemcpy(Cmat->beta_zero, &PETSC_HIPSPARSE_ZERO, sizeof(PetscScalar), hipMemcpyHostT… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2647 …PetscCallHIP(hipMemcpy(Cmat->beta_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpyHostToD… in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2725 PetscCallHIP(hipMalloc((void **)&dBuffer1, bufferSize1)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2730 PetscCallHIP(hipMalloc((void **)&dBuffer2, bufferSize2)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2731 PetscCallHIP(hipMalloc((void **)&dBuffer3, bufferSize3)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2732 PetscCallHIP(hipMalloc((void **)&mmdata->dBuffer4, bufferSize4)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2734 PetscCallHIP(hipFree(dBuffer1)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2735 PetscCallHIP(hipFree(dBuffer2)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2742 PetscCallHIP(hipPeekAtLastError()); /* catch out of memory errors */ in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2744 PetscCallHIP(hipPeekAtLastError()); /* catch out of memory errors */ in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2750 PetscCallHIP(hipMalloc((void **)&mmdata->dBuffer5, bufferSize5)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2752 PetscCallHIP(hipFree(dBuffer3)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2761 PetscCallHIP(hipMalloc((void **)&mmdata->mmBuffer2, bufSize2)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2770 PetscCallHIP(hipMalloc((void **)&mmdata->mmBuffer, mmdata->mmBufferSize)); in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2779 PetscCallHIP(hipPeekAtLastError()); /* catch out of memory errors */ in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2781 PetscCallHIP(hipPeekAtLastError()); /* catch out of memory errors */ in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2791 PetscCallHIP(hipPeekAtLastError()); /* catch out of memory errors */ in MatProductSymbolic_SeqAIJHIPSPARSE_SeqAIJHIPSPARSE()
2793 PetscCallHIP(hipPeekAtLastError()); /* catch out of memory errors */ 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()
3108 …PetscCallHIP(hipMalloc(&matstruct->hipSpMV[opA].spmvBuffer, matstruct->hipSpMV[opA].spmvBufferSize… in MatMultAddKernel_SeqAIJHIPSPARSE()
3304 PetscCallHIP(hipMalloc(&buffer, bufferSize)); in MatAXPY_SeqAIJHIPSPARSE()
3310 PetscCallHIP(hipFree(buffer)); in MatAXPY_SeqAIJHIPSPARSE()
3590 if ((*trifactor)->solveBuffer) PetscCallHIP(hipFree((*trifactor)->solveBuffer)); in MatSeqAIJHIPSPARSEMultStruct_Destroy()
3591 if ((*trifactor)->AA_h) PetscCallHIP(hipHostFree((*trifactor)->AA_h)); in MatSeqAIJHIPSPARSEMultStruct_Destroy()
3592 if ((*trifactor)->csr2cscBuffer) PetscCallHIP(hipFree((*trifactor)->csr2cscBuffer)); in MatSeqAIJHIPSPARSEMultStruct_Destroy()
3615 if ((*matstruct)->alpha_one) PetscCallHIP(hipFree((*matstruct)->alpha_one)); in MatSeqAIJHIPSPARSEMultStruct_Destroy()
3616 if ((*matstruct)->beta_zero) PetscCallHIP(hipFree((*matstruct)->beta_zero)); in MatSeqAIJHIPSPARSEMultStruct_Destroy()
3617 if ((*matstruct)->beta_one) PetscCallHIP(hipFree((*matstruct)->beta_one)); in MatSeqAIJHIPSPARSEMultStruct_Destroy()
3623 PetscCallHIP(hipFree(mdata->hipSpMV[i].spmvBuffer)); in MatSeqAIJHIPSPARSEMultStruct_Destroy()
3652 PetscCallHIP(hipFree(fs->csrRowPtr)); in MatSeqAIJHIPSPARSETriFactors_Reset()
3653 PetscCallHIP(hipFree(fs->csrColIdx)); in MatSeqAIJHIPSPARSETriFactors_Reset()
3654 PetscCallHIP(hipFree(fs->csrVal)); in MatSeqAIJHIPSPARSETriFactors_Reset()
3655 PetscCallHIP(hipFree(fs->X)); in MatSeqAIJHIPSPARSETriFactors_Reset()
3656 PetscCallHIP(hipFree(fs->Y)); in MatSeqAIJHIPSPARSETriFactors_Reset()
3658 PetscCallHIP(hipFree(fs->spsvBuffer_L)); in MatSeqAIJHIPSPARSETriFactors_Reset()
3659 PetscCallHIP(hipFree(fs->spsvBuffer_U)); in MatSeqAIJHIPSPARSETriFactors_Reset()
3660 PetscCallHIP(hipFree(fs->spsvBuffer_Lt)); in MatSeqAIJHIPSPARSETriFactors_Reset()
3661 PetscCallHIP(hipFree(fs->spsvBuffer_Ut)); in MatSeqAIJHIPSPARSETriFactors_Reset()
3724 PetscCallHIP(hipFree(coo->perm)); in MatCOOStructDestroy_SeqAIJHIPSPARSE()
3725 PetscCallHIP(hipFree(coo->jmap)); in MatCOOStructDestroy_SeqAIJHIPSPARSE()
3743 PetscCallHIP(hipMemcpy(i, coo_i, coo_n * sizeof(PetscInt), hipMemcpyDeviceToHost)); in MatSetPreallocationCOO_SeqAIJHIPSPARSE()
3744 PetscCallHIP(hipMemcpy(j, coo_j, coo_n * sizeof(PetscInt), hipMemcpyDeviceToHost)); in MatSetPreallocationCOO_SeqAIJHIPSPARSE()
3760 PetscCallHIP(hipMalloc((void **)&coo_d->jmap, (coo_h->nz + 1) * sizeof(PetscCount))); in MatSetPreallocationCOO_SeqAIJHIPSPARSE()
3761 …PetscCallHIP(hipMemcpy(coo_d->jmap, coo_h->jmap, (coo_h->nz + 1) * sizeof(PetscCount), hipMemcpyHo… in MatSetPreallocationCOO_SeqAIJHIPSPARSE()
3762 PetscCallHIP(hipMalloc((void **)&coo_d->perm, coo_h->Atot * sizeof(PetscCount))); in MatSetPreallocationCOO_SeqAIJHIPSPARSE()
3763 …PetscCallHIP(hipMemcpy(coo_d->perm, coo_h->perm, coo_h->Atot * sizeof(PetscCount), hipMemcpyHostTo… in MatSetPreallocationCOO_SeqAIJHIPSPARSE()
3800 PetscCallHIP(hipMalloc((void **)&v1, coo->n * sizeof(PetscScalar))); in MatSetValuesCOO_SeqAIJHIPSPARSE()
3801 PetscCallHIP(hipMemcpy((void *)v1, v, coo->n * sizeof(PetscScalar), hipMemcpyHostToDevice)); in MatSetValuesCOO_SeqAIJHIPSPARSE()
3810 PetscCallHIP(hipPeekAtLastError()); in MatSetValuesCOO_SeqAIJHIPSPARSE()
3817 if (PetscMemTypeHost(memtype)) PetscCallHIP(hipFree((void *)v1)); in MatSetValuesCOO_SeqAIJHIPSPARSE()
4135 PetscCallHIP(hipMalloc((void **)&Cmat->alpha_one, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEMergeMats()
4136 PetscCallHIP(hipMalloc((void **)&Cmat->beta_zero, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEMergeMats()
4137 PetscCallHIP(hipMalloc((void **)&Cmat->beta_one, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEMergeMats()
4138 …PetscCallHIP(hipMemcpy(Cmat->alpha_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpyHostTo… in MatSeqAIJHIPSPARSEMergeMats()
4139 …PetscCallHIP(hipMemcpy(Cmat->beta_zero, &PETSC_HIPSPARSE_ZERO, sizeof(PetscScalar), hipMemcpyHostT… in MatSeqAIJHIPSPARSEMergeMats()
4140 …PetscCallHIP(hipMemcpy(Cmat->beta_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpyHostToD… in MatSeqAIJHIPSPARSEMergeMats()
4256 PetscCallHIP(hipMalloc((void **)&CmatT->alpha_one, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEMergeMats()
4257 PetscCallHIP(hipMalloc((void **)&CmatT->beta_zero, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEMergeMats()
4258 PetscCallHIP(hipMalloc((void **)&CmatT->beta_one, sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEMergeMats()
4259 …PetscCallHIP(hipMemcpy(CmatT->alpha_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpyHostT… in MatSeqAIJHIPSPARSEMergeMats()
4260 …PetscCallHIP(hipMemcpy(CmatT->beta_zero, &PETSC_HIPSPARSE_ZERO, sizeof(PetscScalar), hipMemcpyHost… in MatSeqAIJHIPSPARSEMergeMats()
4261 …PetscCallHIP(hipMemcpy(CmatT->beta_one, &PETSC_HIPSPARSE_ONE, sizeof(PetscScalar), hipMemcpyHostTo… 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()
4377 …if (w) PetscCallHIP(hipMemcpy(v, w->data().get(), n * sizeof(PetscScalar), hipMemcpyDeviceToHost)); in MatSeqAIJCopySubArray_SeqAIJHIPSPARSE()
4379 …} else PetscCallHIP(hipMemcpy(v, av, n * sizeof(PetscScalar), dmem ? hipMemcpyDeviceToDevice : hip… in MatSeqAIJCopySubArray_SeqAIJHIPSPARSE()