Actual source code: cdiagonal.c

  1: #include <petsc/private/matimpl.h>

  3: typedef struct {
  4:   PetscScalar diag;
  5: } Mat_ConstantDiagonal;

  7: static PetscErrorCode MatAXPY_ConstantDiagonal(Mat Y, PetscScalar a, Mat X, MatStructure str)
  8: {
  9:   Mat_ConstantDiagonal *yctx = (Mat_ConstantDiagonal *)Y->data;
 10:   Mat_ConstantDiagonal *xctx = (Mat_ConstantDiagonal *)X->data;

 12:   PetscFunctionBegin;
 13:   yctx->diag += a * xctx->diag;
 14:   PetscFunctionReturn(PETSC_SUCCESS);
 15: }

 17: static PetscErrorCode MatEqual_ConstantDiagonal(Mat Y, Mat X, PetscBool *equal)
 18: {
 19:   Mat_ConstantDiagonal *yctx = (Mat_ConstantDiagonal *)Y->data;
 20:   Mat_ConstantDiagonal *xctx = (Mat_ConstantDiagonal *)X->data;

 22:   PetscFunctionBegin;
 23:   *equal = (yctx->diag == xctx->diag) ? PETSC_TRUE : PETSC_FALSE;
 24:   PetscFunctionReturn(PETSC_SUCCESS);
 25: }

 27: static PetscErrorCode MatGetRow_ConstantDiagonal(Mat A, PetscInt row, PetscInt *ncols, PetscInt *cols[], PetscScalar *vals[])
 28: {
 29:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)A->data;

 31:   PetscFunctionBegin;
 32:   if (ncols) *ncols = 1;
 33:   if (cols) {
 34:     PetscCall(PetscMalloc1(1, cols));
 35:     (*cols)[0] = row;
 36:   }
 37:   if (vals) {
 38:     PetscCall(PetscMalloc1(1, vals));
 39:     (*vals)[0] = ctx->diag;
 40:   }
 41:   PetscFunctionReturn(PETSC_SUCCESS);
 42: }

 44: static PetscErrorCode MatRestoreRow_ConstantDiagonal(Mat A, PetscInt row, PetscInt *ncols, PetscInt *cols[], PetscScalar *vals[])
 45: {
 46:   PetscFunctionBegin;
 47:   if (cols) PetscCall(PetscFree(*cols));
 48:   if (vals) PetscCall(PetscFree(*vals));
 49:   PetscFunctionReturn(PETSC_SUCCESS);
 50: }

 52: static PetscErrorCode MatMultAdd_ConstantDiagonal(Mat mat, Vec v1, Vec v2, Vec v3)
 53: {
 54:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)mat->data;

 56:   PetscFunctionBegin;
 57:   if (v2 == v3) PetscCall(VecAXPBY(v3, ctx->diag, 1.0, v1));
 58:   else PetscCall(VecAXPBYPCZ(v3, ctx->diag, 1.0, 0.0, v1, v2));
 59:   PetscFunctionReturn(PETSC_SUCCESS);
 60: }

 62: static PetscErrorCode MatMultHermitianTransposeAdd_ConstantDiagonal(Mat mat, Vec v1, Vec v2, Vec v3)
 63: {
 64:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)mat->data;

 66:   PetscFunctionBegin;
 67:   if (v2 == v3) PetscCall(VecAXPBY(v3, PetscConj(ctx->diag), 1.0, v1));
 68:   else PetscCall(VecAXPBYPCZ(v3, PetscConj(ctx->diag), 1.0, 0.0, v1, v2));
 69:   PetscFunctionReturn(PETSC_SUCCESS);
 70: }

 72: static PetscErrorCode MatNorm_ConstantDiagonal(Mat A, NormType type, PetscReal *nrm)
 73: {
 74:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)A->data;

 76:   PetscFunctionBegin;
 77:   PetscCheck(type == NORM_FROBENIUS || type == NORM_2 || type == NORM_1 || type == NORM_INFINITY, PetscObjectComm((PetscObject)A), PETSC_ERR_SUP, "Unsupported norm");
 78:   *nrm = PetscAbsScalar(ctx->diag);
 79:   PetscFunctionReturn(PETSC_SUCCESS);
 80: }

 82: static PetscErrorCode MatCreateSubMatrices_ConstantDiagonal(Mat A, PetscInt n, const IS irow[], const IS icol[], MatReuse scall, Mat *submat[])
 83: {
 84:   Mat B;

 86:   PetscFunctionBegin;
 87:   PetscCall(MatConvert(A, MATAIJ, MAT_INITIAL_MATRIX, &B));
 88:   PetscCall(MatCreateSubMatrices(B, n, irow, icol, scall, submat));
 89:   PetscCall(MatDestroy(&B));
 90:   PetscFunctionReturn(PETSC_SUCCESS);
 91: }

 93: static PetscErrorCode MatDuplicate_ConstantDiagonal(Mat A, MatDuplicateOption op, Mat *B)
 94: {
 95:   Mat_ConstantDiagonal *actx = (Mat_ConstantDiagonal *)A->data;

 97:   PetscFunctionBegin;
 98:   PetscCall(MatCreate(PetscObjectComm((PetscObject)A), B));
 99:   PetscCall(MatSetSizes(*B, A->rmap->n, A->cmap->n, A->rmap->N, A->cmap->N));
100:   PetscCall(MatSetBlockSizesFromMats(*B, A, A));
101:   PetscCall(MatSetType(*B, MATCONSTANTDIAGONAL));
102:   PetscCall(PetscLayoutReference(A->rmap, &(*B)->rmap));
103:   PetscCall(PetscLayoutReference(A->cmap, &(*B)->cmap));
104:   if (op == MAT_COPY_VALUES) {
105:     Mat_ConstantDiagonal *bctx = (Mat_ConstantDiagonal *)(*B)->data;
106:     bctx->diag                 = actx->diag;
107:   }
108:   PetscFunctionReturn(PETSC_SUCCESS);
109: }

111: static PetscErrorCode MatDestroy_ConstantDiagonal(Mat mat)
112: {
113:   PetscFunctionBegin;
114:   PetscCall(PetscFree(mat->data));
115:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatConstantDiagonalGetConstant_C", NULL));
116:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_constantdiagonal_constantdiagonal_C", NULL));
117:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_constantdiagonal_diagonal_C", NULL));
118:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_diagonal_constantdiagonal_C", NULL));
119:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_constantdiagonal_seqdense_C", NULL));
120:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_constantdiagonal_mpidense_C", NULL));
121: #if PetscDefined(HAVE_CUDA)
122:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_constantdiagonal_seqdensecuda_C", NULL));
123:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_constantdiagonal_mpidensecuda_C", NULL));
124: #endif
125: #if PetscDefined(HAVE_HIP)
126:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_constantdiagonal_seqdensehip_C", NULL));
127:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_constantdiagonal_mpidensehip_C", NULL));
128: #endif
129:   PetscCall(PetscObjectComposeFunction((PetscObject)mat, "MatProductSetFromOptions_anytype_C", NULL));
130:   PetscFunctionReturn(PETSC_SUCCESS);
131: }

133: static PetscErrorCode MatView_ConstantDiagonal(Mat J, PetscViewer viewer)
134: {
135:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)J->data;
136:   PetscBool             isascii;

138:   PetscFunctionBegin;
139:   PetscCall(PetscObjectTypeCompare((PetscObject)viewer, PETSCVIEWERASCII, &isascii));
140:   if (isascii) {
141:     PetscViewerFormat format;

143:     PetscCall(PetscViewerGetFormat(viewer, &format));
144:     if (format == PETSC_VIEWER_ASCII_FACTOR_INFO || format == PETSC_VIEWER_ASCII_INFO) PetscFunctionReturn(PETSC_SUCCESS);
145:     if (PetscImaginaryPart(ctx->diag) == 0) {
146:       PetscCall(PetscViewerASCIIPrintf(viewer, "Diagonal value: %g\n", (double)PetscRealPart(ctx->diag)));
147:     } else {
148:       PetscCall(PetscViewerASCIIPrintf(viewer, "Diagonal value: %g + i %g\n", (double)PetscRealPart(ctx->diag), (double)PetscImaginaryPart(ctx->diag)));
149:     }
150:   }
151:   PetscFunctionReturn(PETSC_SUCCESS);
152: }

154: static PetscErrorCode MatMult_ConstantDiagonal(Mat J, Vec x, Vec y)
155: {
156:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)J->data;

158:   PetscFunctionBegin;
159:   PetscCall(VecAXPBY(y, ctx->diag, 0.0, x));
160:   PetscFunctionReturn(PETSC_SUCCESS);
161: }

163: static PetscErrorCode MatMultHermitianTranspose_ConstantDiagonal(Mat J, Vec x, Vec y)
164: {
165:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)J->data;

167:   PetscFunctionBegin;
168:   PetscCall(VecAXPBY(y, PetscConj(ctx->diag), 0.0, x));
169:   PetscFunctionReturn(PETSC_SUCCESS);
170: }

172: static PetscErrorCode MatGetDiagonal_ConstantDiagonal(Mat J, Vec x)
173: {
174:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)J->data;

176:   PetscFunctionBegin;
177:   PetscCall(VecSet(x, ctx->diag));
178:   PetscFunctionReturn(PETSC_SUCCESS);
179: }

181: static PetscErrorCode MatShift_ConstantDiagonal(Mat Y, PetscScalar a)
182: {
183:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)Y->data;

185:   PetscFunctionBegin;
186:   ctx->diag += a;
187:   PetscFunctionReturn(PETSC_SUCCESS);
188: }

190: static PetscErrorCode MatScale_ConstantDiagonal(Mat Y, PetscScalar a)
191: {
192:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)Y->data;

194:   PetscFunctionBegin;
195:   ctx->diag *= a;
196:   PetscFunctionReturn(PETSC_SUCCESS);
197: }

199: static PetscErrorCode MatZeroEntries_ConstantDiagonal(Mat Y)
200: {
201:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)Y->data;

203:   PetscFunctionBegin;
204:   ctx->diag = 0.0;
205:   PetscFunctionReturn(PETSC_SUCCESS);
206: }

208: static PetscErrorCode MatConjugate_ConstantDiagonal(Mat Y)
209: {
210:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)Y->data;

212:   PetscFunctionBegin;
213:   ctx->diag = PetscConj(ctx->diag);
214:   PetscFunctionReturn(PETSC_SUCCESS);
215: }

217: static PetscErrorCode MatTranspose_ConstantDiagonal(Mat A, MatReuse reuse, Mat *matout)
218: {
219:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)A->data;

221:   PetscFunctionBegin;
222:   if (reuse == MAT_INPLACE_MATRIX) {
223:     PetscLayout tmplayout = A->rmap;

225:     A->rmap = A->cmap;
226:     A->cmap = tmplayout;
227:   } else {
228:     if (reuse == MAT_INITIAL_MATRIX) {
229:       PetscCall(MatCreateConstantDiagonal(PetscObjectComm((PetscObject)A), A->cmap->n, A->rmap->n, A->cmap->N, A->rmap->N, ctx->diag, matout));
230:     } else {
231:       PetscCall(MatZeroEntries(*matout));
232:       PetscCall(MatShift(*matout, ctx->diag));
233:     }
234:   }
235:   PetscFunctionReturn(PETSC_SUCCESS);
236: }

238: static PetscErrorCode MatSetRandom_ConstantDiagonal(Mat A, PetscRandom rand)
239: {
240:   PetscMPIInt           rank;
241:   MPI_Comm              comm;
242:   PetscScalar           v   = 0.0;
243:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)A->data;

245:   PetscFunctionBegin;
246:   PetscCall(PetscObjectGetComm((PetscObject)A, &comm));
247:   PetscCallMPI(MPI_Comm_rank(comm, &rank));
248:   if (!rank) PetscCall(PetscRandomGetValue(rand, &v));
249:   PetscCallMPI(MPI_Bcast(&v, 1, MPIU_SCALAR, 0, comm));
250:   ctx->diag = v;
251:   PetscFunctionReturn(PETSC_SUCCESS);
252: }

254: static PetscErrorCode MatSolve_ConstantDiagonal(Mat matin, Vec b, Vec x)
255: {
256:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)matin->data;

258:   PetscFunctionBegin;
259:   if (ctx->diag == 0.0) matin->factorerrortype = MAT_FACTOR_NUMERIC_ZEROPIVOT;
260:   else matin->factorerrortype = MAT_FACTOR_NOERROR;
261:   PetscCall(VecAXPBY(x, 1.0 / ctx->diag, 0.0, b));
262:   PetscFunctionReturn(PETSC_SUCCESS);
263: }

265: static PetscErrorCode MatSOR_ConstantDiagonal(Mat matin, Vec x, PetscReal omega, MatSORType flag, PetscReal fshift, PetscInt its, PetscInt lits, Vec y)
266: {
267:   PetscFunctionBegin;
268:   PetscCall(MatSolve_ConstantDiagonal(matin, x, y));
269:   PetscFunctionReturn(PETSC_SUCCESS);
270: }

272: static PetscErrorCode MatGetInfo_ConstantDiagonal(Mat A, MatInfoType flag, MatInfo *info)
273: {
274:   PetscFunctionBegin;
275:   info->block_size   = 1.0;
276:   info->nz_allocated = 1.0;
277:   info->nz_used      = 1.0;
278:   info->nz_unneeded  = 0.0;
279:   info->assemblies   = A->num_ass;
280:   info->mallocs      = 0.0;
281:   info->memory       = 0; /* REVIEW ME */
282:   if (A->factortype) {
283:     info->fill_ratio_given  = 1.0;
284:     info->fill_ratio_needed = 1.0;
285:     info->factor_mallocs    = 0.0;
286:   } else {
287:     info->fill_ratio_given  = 0;
288:     info->fill_ratio_needed = 0;
289:     info->factor_mallocs    = 0;
290:   }
291:   PetscFunctionReturn(PETSC_SUCCESS);
292: }

294: /*@
295:   MatCreateConstantDiagonal - Creates a matrix with a uniform value along the diagonal

297:   Collective

299:   Input Parameters:
300: + comm - MPI communicator
301: . m    - number of local rows (or `PETSC_DECIDE` to have calculated if `M` is given)
302:            This value should be the same as the local size used in creating the
303:            y vector for the matrix-vector product y = Ax.
304: . n    - This value should be the same as the local size used in creating the
305:        x vector for the matrix-vector product y = Ax. (or `PETSC_DECIDE` to have
306:        calculated if `N` is given) For square matrices n is almost always `m`.
307: . M    - number of global rows (or `PETSC_DETERMINE` to have calculated if m is given)
308: . N    - number of global columns (or `PETSC_DETERMINE` to have calculated if n is given)
309: - diag - the diagonal value

311:   Output Parameter:
312: . J - the diagonal matrix

314:   Level: advanced

316:   Notes:
317:   Only supports square matrices with the same number of local rows and columns

319: .seealso: [](ch_matrices), `Mat`, `MatDestroy()`, `MATCONSTANTDIAGONAL`, `MatScale()`, `MatShift()`, `MatMult()`, `MatGetDiagonal()`, `MatGetFactor()`, `MatSolve()`
320: @*/
321: PetscErrorCode MatCreateConstantDiagonal(MPI_Comm comm, PetscInt m, PetscInt n, PetscInt M, PetscInt N, PetscScalar diag, Mat *J)
322: {
323:   PetscFunctionBegin;
324:   PetscCall(MatCreate(comm, J));
325:   PetscCall(MatSetSizes(*J, m, n, M, N));
326:   PetscCall(MatSetType(*J, MATCONSTANTDIAGONAL));
327:   PetscCall(MatShift(*J, diag));
328:   PetscCall(MatSetUp(*J));
329:   PetscFunctionReturn(PETSC_SUCCESS);
330: }

332: /*@
333:   MatConstantDiagonalGetConstant - Get the scalar constant of a constant diagonal matrix

335:   Not collective

337:   Input Parameter:
338: . mat - a `MATCONSTANTDIAGONAL`

340:   Output Parameter:
341: . value - the scalar value

343:   Level: developer

345: .seealso: [](ch_matrices), `Mat`, `MatDestroy()`, `MATCONSTANTDIAGONAL`
346: @*/
347: PetscErrorCode MatConstantDiagonalGetConstant(Mat mat, PetscScalar *value)
348: {
349:   PetscFunctionBegin;
350:   PetscUseMethod(mat, "MatConstantDiagonalGetConstant_C", (Mat, PetscScalar *), (mat, value));
351:   PetscFunctionReturn(PETSC_SUCCESS);
352: }

354: static PetscErrorCode MatConstantDiagonalGetConstant_ConstantDiagonal(Mat mat, PetscScalar *value)
355: {
356:   Mat_ConstantDiagonal *ctx = (Mat_ConstantDiagonal *)mat->data;

358:   PetscFunctionBegin;
359:   *value = ctx->diag;
360:   PetscFunctionReturn(PETSC_SUCCESS);
361: }

363: static PetscErrorCode MatProductNumeric_ConstDiag_Dense(Mat C)
364: {
365:   Mat_ConstantDiagonal *p = (Mat_ConstantDiagonal *)C->product->A->data;

367:   PetscFunctionBegin;
368:   MatCheckProduct(C, 1);
369:   PetscCall(MatCopy(C->product->B, C, SAME_NONZERO_PATTERN));
370:   PetscCall(MatScale(C, p->diag));
371:   PetscFunctionReturn(PETSC_SUCCESS);
372: }

374: static PetscErrorCode MatProductSymbolic_ConstDiag_Dense(Mat C)
375: {
376:   Mat      A, B;
377:   PetscInt n, N, m, M;

379:   PetscFunctionBegin;
380:   MatCheckProduct(C, 1);
381:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
382:   A = C->product->A;
383:   B = C->product->B;
384:   PetscCall(MatGetLocalSize(B, NULL, &n));
385:   PetscCall(MatGetSize(B, NULL, &N));
386:   PetscCall(MatGetLocalSize(A, &m, NULL));
387:   PetscCall(MatGetSize(A, &M, NULL));
388:   PetscCall(MatSetSizes(C, m, n, M, N));
389:   PetscCall(MatSetType(C, ((PetscObject)B)->type_name));
390:   PetscCall(MatSetUp(C));
391:   C->ops->productnumeric = MatProductNumeric_ConstDiag_Dense;
392:   PetscFunctionReturn(PETSC_SUCCESS);
393: }

395: /* PtAP for constantdiagonal * constantdiagonal: C = alpha * beta^2 * I */
396: static PetscErrorCode MatProductNumeric_PtAP_ConstDiag_ConstDiag(Mat C)
397: {
398:   Mat                   A = C->product->A, P = C->product->B;
399:   Mat_ConstantDiagonal *a = (Mat_ConstantDiagonal *)A->data, *p = (Mat_ConstantDiagonal *)P->data, *c = (Mat_ConstantDiagonal *)C->data;

401:   PetscFunctionBegin;
402:   MatCheckProduct(C, 1);
403:   c->diag = a->diag * p->diag * p->diag;
404:   PetscFunctionReturn(PETSC_SUCCESS);
405: }

407: static PetscErrorCode MatProductSymbolic_PtAP_ConstDiag_ConstDiag(Mat C)
408: {
409:   Mat P = C->product->B;

411:   PetscFunctionBegin;
412:   MatCheckProduct(C, 1);
413:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
414:   PetscCall(MatSetSizes(C, P->cmap->n, P->cmap->n, P->cmap->N, P->cmap->N));
415:   PetscCall(MatSetType(C, MATCONSTANTDIAGONAL));
416:   C->assembled           = PETSC_TRUE;
417:   C->ops->productnumeric = MatProductNumeric_PtAP_ConstDiag_ConstDiag;
418:   PetscFunctionReturn(PETSC_SUCCESS);
419: }

421: /* PtAP for constantdiagonal A and diagonal P: C_i = alpha * p_i^2 */
422: static PetscErrorCode MatProductNumeric_PtAP_ConstDiag_Diagonal(Mat C)
423: {
424:   Mat                   A = C->product->A, P = C->product->B;
425:   Mat_ConstantDiagonal *a = (Mat_ConstantDiagonal *)A->data;
426:   Vec                   pdiag, cdiag;

428:   PetscFunctionBegin;
429:   MatCheckProduct(C, 1);
430:   PetscCall(MatDiagonalGetDiagonal(P, &pdiag));
431:   PetscCall(MatDiagonalGetDiagonal(C, &cdiag));
432:   PetscCall(VecPointwiseMult(cdiag, pdiag, pdiag));
433:   PetscCall(VecScale(cdiag, a->diag));
434:   PetscCall(MatDiagonalRestoreDiagonal(C, &cdiag));
435:   PetscCall(MatDiagonalRestoreDiagonal(P, &pdiag));
436:   PetscFunctionReturn(PETSC_SUCCESS);
437: }

439: static PetscErrorCode MatProductSymbolic_PtAP_ConstDiag_Diagonal(Mat C)
440: {
441:   Mat P = C->product->B;
442:   Vec pdiag, cdiag;

444:   PetscFunctionBegin;
445:   MatCheckProduct(C, 1);
446:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
447:   PetscCall(MatSetSizes(C, P->cmap->n, P->cmap->n, P->cmap->N, P->cmap->N));
448:   PetscCall(MatSetType(C, MATDIAGONAL));
449:   PetscCall(MatDiagonalGetDiagonal(P, &pdiag));
450:   PetscCall(VecDuplicate(pdiag, &cdiag));
451:   PetscCall(MatDiagonalSetDiagonal(C, cdiag));
452:   PetscCall(VecDestroy(&cdiag));
453:   PetscCall(MatDiagonalRestoreDiagonal(P, &pdiag));
454:   C->assembled           = PETSC_TRUE;
455:   C->ops->productnumeric = MatProductNumeric_PtAP_ConstDiag_Diagonal;
456:   PetscFunctionReturn(PETSC_SUCCESS);
457: }

459: /* PtAP for diagonal A and constantdiagonal P: C_i = beta^2 * a_i */
460: static PetscErrorCode MatProductNumeric_PtAP_Diagonal_ConstDiag(Mat C)
461: {
462:   Mat                   A = C->product->A, P = C->product->B;
463:   Mat_ConstantDiagonal *p = (Mat_ConstantDiagonal *)P->data;
464:   Vec                   adiag, cdiag;

466:   PetscFunctionBegin;
467:   MatCheckProduct(C, 1);
468:   PetscCall(MatDiagonalGetDiagonal(A, &adiag));
469:   PetscCall(MatDiagonalGetDiagonal(C, &cdiag));
470:   PetscCall(VecCopy(adiag, cdiag));
471:   PetscCall(VecScale(cdiag, p->diag * p->diag));
472:   PetscCall(MatDiagonalRestoreDiagonal(C, &cdiag));
473:   PetscCall(MatDiagonalRestoreDiagonal(A, &adiag));
474:   PetscFunctionReturn(PETSC_SUCCESS);
475: }

477: static PetscErrorCode MatProductSymbolic_PtAP_Diagonal_ConstDiag(Mat C)
478: {
479:   Mat A = C->product->A, P = C->product->B;
480:   Vec adiag, cdiag;

482:   PetscFunctionBegin;
483:   MatCheckProduct(C, 1);
484:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
485:   PetscCall(MatSetSizes(C, P->cmap->n, P->cmap->n, P->cmap->N, P->cmap->N));
486:   PetscCall(MatSetType(C, MATDIAGONAL));
487:   /* Duplicate A's diagonal Vec so C inherits the correct VecType (e.g., Kokkos, CUDA, HIP) */
488:   PetscCall(MatDiagonalGetDiagonal(A, &adiag));
489:   PetscCall(VecDuplicate(adiag, &cdiag));
490:   PetscCall(MatDiagonalSetDiagonal(C, cdiag));
491:   PetscCall(VecDestroy(&cdiag));
492:   PetscCall(MatDiagonalRestoreDiagonal(A, &adiag));
493:   C->assembled           = PETSC_TRUE;
494:   C->ops->productnumeric = MatProductNumeric_PtAP_Diagonal_ConstDiag;
495:   PetscFunctionReturn(PETSC_SUCCESS);
496: }

498: /* PtAP for any (non-diagonal) A and constantdiagonal P: C = beta^2 * A */
499: static PetscErrorCode MatProductNumeric_PtAP_Anytype_ConstDiag(Mat C)
500: {
501:   Mat                   A = C->product->A, P = C->product->B;
502:   Mat_ConstantDiagonal *p = (Mat_ConstantDiagonal *)P->data;

504:   PetscFunctionBegin;
505:   MatCheckProduct(C, 1);
506:   PetscCall(MatCopy(A, C, SAME_NONZERO_PATTERN));
507:   PetscCall(MatScale(C, p->diag * p->diag));
508:   PetscFunctionReturn(PETSC_SUCCESS);
509: }

511: static PetscErrorCode MatProductSymbolic_PtAP_Anytype_ConstDiag(Mat C)
512: {
513:   Mat          A       = C->product->A;
514:   Mat_Product *product = C->product;
515:   Mat          Cwork;

517:   PetscFunctionBegin;
518:   MatCheckProduct(C, 1);
519:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
520:   PetscCall(MatDuplicate(A, MAT_DO_NOT_COPY_VALUES, &Cwork));
521:   C->product = NULL;
522:   PetscCall(MatHeaderReplace(C, &Cwork));
523:   C->product             = product;
524:   C->ops->productnumeric = MatProductNumeric_PtAP_Anytype_ConstDiag;
525:   PetscFunctionReturn(PETSC_SUCCESS);
526: }

528: /* PtAP for constantdiagonal A and any non-diagonal P: C = alpha * P^T * P */
529: typedef struct {
530:   Mat              PtP;       /* P^T * P result via MatProduct AtB */
531:   PetscObjectState pnnzstate; /* P's nonzero state when inner symbolic was last built */
532: } MatProductCtx_PtAP_ConstDiag_Anytype;

534: static PetscErrorCode MatProductCtxDestroy_PtAP_ConstDiag_Anytype(PetscCtxRt data)
535: {
536:   MatProductCtx_PtAP_ConstDiag_Anytype *ctx = *(MatProductCtx_PtAP_ConstDiag_Anytype **)data;

538:   PetscFunctionBegin;
539:   PetscCall(MatDestroy(&ctx->PtP));
540:   PetscCall(PetscFree(ctx));
541:   PetscFunctionReturn(PETSC_SUCCESS);
542: }

544: static PetscErrorCode MatProductNumeric_PtAP_ConstDiag_Anytype(Mat C)
545: {
546:   Mat_Product                          *product = C->product;
547:   Mat                                   A = product->A, P = product->B;
548:   MatProductCtx_PtAP_ConstDiag_Anytype *ctx = (MatProductCtx_PtAP_ConstDiag_Anytype *)product->data;
549:   Mat_ConstantDiagonal                 *a   = (Mat_ConstantDiagonal *)A->data;
550:   PetscObjectState                      pnnzstate;

552:   PetscFunctionBegin;
553:   MatCheckProduct(C, 1);
554:   /* Rebuild inner symbolic if P's nonzero structure has changed */
555:   PetscCall(MatGetNonzeroState(P, &pnnzstate));
556:   if (pnnzstate != ctx->pnnzstate) {
557:     PetscCall(MatDestroy(&ctx->PtP));
558:     PetscCall(MatProductCreate(P, P, NULL, &ctx->PtP));
559:     PetscCall(MatProductSetType(ctx->PtP, MATPRODUCT_AtB));
560:     PetscCall(MatProductSetFill(ctx->PtP, product->fill));
561:     PetscCall(MatProductSetFromOptions(ctx->PtP));
562:     PetscCall(MatProductSymbolic(ctx->PtP));
563:     ctx->pnnzstate = pnnzstate;
564:   }
565:   /* Compute P^T * P */
566:   PetscCall(MatProductNumeric(ctx->PtP));
567:   PetscCall(MatCopy(ctx->PtP, C, SAME_NONZERO_PATTERN));
568:   PetscCall(MatScale(C, a->diag));
569:   PetscFunctionReturn(PETSC_SUCCESS);
570: }

572: static PetscErrorCode MatProductSymbolic_PtAP_ConstDiag_Anytype(Mat C)
573: {
574:   Mat_Product                          *product = C->product;
575:   Mat                                   P       = product->B;
576:   MatProductCtx_PtAP_ConstDiag_Anytype *ctx;
577:   Mat                                   Cwork;

579:   PetscFunctionBegin;
580:   MatCheckProduct(C, 1);
581:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
582:   PetscCall(PetscNew(&ctx));

584:   /* PtP = P^T * P (symbolic) */
585:   PetscCall(MatProductCreate(P, P, NULL, &ctx->PtP));
586:   PetscCall(MatProductSetType(ctx->PtP, MATPRODUCT_AtB));
587:   PetscCall(MatProductSetFill(ctx->PtP, product->fill));
588:   PetscCall(MatProductSetFromOptions(ctx->PtP));
589:   PetscCall(MatProductSymbolic(ctx->PtP));

591:   /* Record P's nonzero state so numeric phase can detect structural changes */
592:   PetscCall(MatGetNonzeroState(P, &ctx->pnnzstate));

594:   /* Set up C with the same structure as PtP */
595:   PetscCall(MatDuplicate(ctx->PtP, MAT_DO_NOT_COPY_VALUES, &Cwork));
596:   C->product = NULL;
597:   PetscCall(MatHeaderReplace(C, &Cwork));
598:   C->product = product;
599:   PetscCall(MatSetOption(C, MAT_NO_OFF_PROC_ENTRIES, PETSC_TRUE));
600:   PetscCall(MatAssemblyBegin(C, MAT_FINAL_ASSEMBLY));
601:   PetscCall(MatAssemblyEnd(C, MAT_FINAL_ASSEMBLY));
602:   product->data          = ctx;
603:   product->destroy       = MatProductCtxDestroy_PtAP_ConstDiag_Anytype;
604:   C->ops->productnumeric = MatProductNumeric_PtAP_ConstDiag_Anytype;
605:   PetscFunctionReturn(PETSC_SUCCESS);
606: }

608: /* AB for MATCONSTANTDIAGONAL A and any non-diagonal B: C = alpha * B */
609: static PetscErrorCode MatProductNumeric_AB_ConstDiag_Anytype(Mat C)
610: {
611:   Mat                   A = C->product->A, B = C->product->B;
612:   Mat_ConstantDiagonal *a = (Mat_ConstantDiagonal *)A->data;

614:   PetscFunctionBegin;
615:   MatCheckProduct(C, 1);
616:   PetscCall(MatCopy(B, C, SAME_NONZERO_PATTERN));
617:   PetscCall(MatScale(C, a->diag));
618:   PetscFunctionReturn(PETSC_SUCCESS);
619: }

621: static PetscErrorCode MatProductSymbolic_AB_ConstDiag_Anytype(Mat C)
622: {
623:   Mat          B       = C->product->B;
624:   Mat_Product *product = C->product;
625:   Mat          Cwork;

627:   PetscFunctionBegin;
628:   MatCheckProduct(C, 1);
629:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
630:   PetscCall(MatDuplicate(B, MAT_DO_NOT_COPY_VALUES, &Cwork));
631:   C->product = NULL;
632:   PetscCall(MatHeaderReplace(C, &Cwork));
633:   C->product             = product;
634:   C->ops->productnumeric = MatProductNumeric_AB_ConstDiag_Anytype;
635:   PetscFunctionReturn(PETSC_SUCCESS);
636: }

638: /* AB for any non-diagonal A and MATCONSTANTDIAGONAL B: C = beta * A */
639: static PetscErrorCode MatProductNumeric_AB_Anytype_ConstDiag(Mat C)
640: {
641:   Mat                   A = C->product->A, B = C->product->B;
642:   Mat_ConstantDiagonal *b = (Mat_ConstantDiagonal *)B->data;

644:   PetscFunctionBegin;
645:   MatCheckProduct(C, 1);
646:   PetscCall(MatCopy(A, C, SAME_NONZERO_PATTERN));
647:   PetscCall(MatScale(C, b->diag));
648:   PetscFunctionReturn(PETSC_SUCCESS);
649: }

651: static PetscErrorCode MatProductSymbolic_AB_Anytype_ConstDiag(Mat C)
652: {
653:   Mat          A       = C->product->A;
654:   Mat_Product *product = C->product;
655:   Mat          Cwork;

657:   PetscFunctionBegin;
658:   MatCheckProduct(C, 1);
659:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
660:   PetscCall(MatDuplicate(A, MAT_DO_NOT_COPY_VALUES, &Cwork));
661:   C->product = NULL;
662:   PetscCall(MatHeaderReplace(C, &Cwork));
663:   C->product             = product;
664:   C->ops->productnumeric = MatProductNumeric_AB_Anytype_ConstDiag;
665:   PetscFunctionReturn(PETSC_SUCCESS);
666: }

668: /* AB for MATCONSTANTDIAGONAL * MATCONSTANTDIAGONAL: C = alpha * beta * I */
669: static PetscErrorCode MatProductNumeric_AB_ConstDiag_ConstDiag(Mat C)
670: {
671:   Mat                   A = C->product->A, B = C->product->B;
672:   Mat_ConstantDiagonal *a = (Mat_ConstantDiagonal *)A->data, *b = (Mat_ConstantDiagonal *)B->data, *c = (Mat_ConstantDiagonal *)C->data;

674:   PetscFunctionBegin;
675:   MatCheckProduct(C, 1);
676:   c->diag = a->diag * b->diag;
677:   PetscFunctionReturn(PETSC_SUCCESS);
678: }

680: static PetscErrorCode MatProductSymbolic_AB_ConstDiag_ConstDiag(Mat C)
681: {
682:   Mat A = C->product->A, B = C->product->B;

684:   PetscFunctionBegin;
685:   MatCheckProduct(C, 1);
686:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
687:   PetscCall(MatSetSizes(C, A->rmap->n, B->cmap->n, A->rmap->N, B->cmap->N));
688:   PetscCall(MatSetType(C, MATCONSTANTDIAGONAL));
689:   C->assembled           = PETSC_TRUE;
690:   C->ops->productnumeric = MatProductNumeric_AB_ConstDiag_ConstDiag;
691:   PetscFunctionReturn(PETSC_SUCCESS);
692: }

694: /* AB for MATCONSTANTDIAGONAL A and MATDIAGONAL B: C_i = alpha * b_i */
695: static PetscErrorCode MatProductNumeric_AB_ConstDiag_Diagonal(Mat C)
696: {
697:   Mat                   A = C->product->A, B = C->product->B;
698:   Mat_ConstantDiagonal *a = (Mat_ConstantDiagonal *)A->data;
699:   Vec                   bdiag, cdiag;

701:   PetscFunctionBegin;
702:   MatCheckProduct(C, 1);
703:   PetscCall(MatDiagonalGetDiagonal(B, &bdiag));
704:   PetscCall(MatDiagonalGetDiagonal(C, &cdiag));
705:   PetscCall(VecCopy(bdiag, cdiag));
706:   PetscCall(VecScale(cdiag, a->diag));
707:   PetscCall(MatDiagonalRestoreDiagonal(C, &cdiag));
708:   PetscCall(MatDiagonalRestoreDiagonal(B, &bdiag));
709:   PetscFunctionReturn(PETSC_SUCCESS);
710: }

712: static PetscErrorCode MatProductSymbolic_AB_ConstDiag_Diagonal(Mat C)
713: {
714:   Mat A = C->product->A, B = C->product->B;
715:   Vec bdiag, cdiag;

717:   PetscFunctionBegin;
718:   MatCheckProduct(C, 1);
719:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
720:   PetscCall(MatSetSizes(C, A->rmap->n, B->cmap->n, A->rmap->N, B->cmap->N));
721:   PetscCall(MatSetType(C, MATDIAGONAL));
722:   /* Duplicate B's diagonal Vec so C inherits the correct VecType (e.g., Kokkos, CUDA, HIP) */
723:   PetscCall(MatDiagonalGetDiagonal(B, &bdiag));
724:   PetscCall(VecDuplicate(bdiag, &cdiag));
725:   PetscCall(MatDiagonalSetDiagonal(C, cdiag));
726:   PetscCall(VecDestroy(&cdiag));
727:   PetscCall(MatDiagonalRestoreDiagonal(B, &bdiag));
728:   C->assembled           = PETSC_TRUE;
729:   C->ops->productnumeric = MatProductNumeric_AB_ConstDiag_Diagonal;
730:   PetscFunctionReturn(PETSC_SUCCESS);
731: }

733: /* AB for MATDIAGONAL A and MATCONSTANTDIAGONAL B: C_i = beta * a_i */
734: static PetscErrorCode MatProductNumeric_AB_Diagonal_ConstDiag(Mat C)
735: {
736:   Mat                   A = C->product->A, B = C->product->B;
737:   Mat_ConstantDiagonal *b = (Mat_ConstantDiagonal *)B->data;
738:   Vec                   adiag, cdiag;

740:   PetscFunctionBegin;
741:   MatCheckProduct(C, 1);
742:   PetscCall(MatDiagonalGetDiagonal(A, &adiag));
743:   PetscCall(MatDiagonalGetDiagonal(C, &cdiag));
744:   PetscCall(VecCopy(adiag, cdiag));
745:   PetscCall(VecScale(cdiag, b->diag));
746:   PetscCall(MatDiagonalRestoreDiagonal(C, &cdiag));
747:   PetscCall(MatDiagonalRestoreDiagonal(A, &adiag));
748:   PetscFunctionReturn(PETSC_SUCCESS);
749: }

751: static PetscErrorCode MatProductSymbolic_AB_Diagonal_ConstDiag(Mat C)
752: {
753:   Mat A = C->product->A, B = C->product->B;
754:   Vec adiag, cdiag;

756:   PetscFunctionBegin;
757:   MatCheckProduct(C, 1);
758:   PetscCheck(!C->product->data, PetscObjectComm((PetscObject)C), PETSC_ERR_PLIB, "Product data not empty");
759:   PetscCall(MatSetSizes(C, A->rmap->n, B->cmap->n, A->rmap->N, B->cmap->N));
760:   PetscCall(MatSetType(C, MATDIAGONAL));
761:   /* Duplicate A's diagonal Vec so C inherits the correct VecType (e.g., Kokkos, CUDA, HIP) */
762:   PetscCall(MatDiagonalGetDiagonal(A, &adiag));
763:   PetscCall(VecDuplicate(adiag, &cdiag));
764:   PetscCall(MatDiagonalSetDiagonal(C, cdiag));
765:   PetscCall(VecDestroy(&cdiag));
766:   PetscCall(MatDiagonalRestoreDiagonal(A, &adiag));
767:   C->assembled           = PETSC_TRUE;
768:   C->ops->productnumeric = MatProductNumeric_AB_Diagonal_ConstDiag;
769:   PetscFunctionReturn(PETSC_SUCCESS);
770: }

772: static PetscErrorCode MatProductSetFromOptions_ConstDiag_ConstDiag(Mat C)
773: {
774:   Mat_Product *product = C->product;

776:   PetscFunctionBegin;
777:   if (product->type == MATPRODUCT_PtAP) C->ops->productsymbolic = MatProductSymbolic_PtAP_ConstDiag_ConstDiag;
778:   else if (product->type == MATPRODUCT_AB) C->ops->productsymbolic = MatProductSymbolic_AB_ConstDiag_ConstDiag;
779:   PetscFunctionReturn(PETSC_SUCCESS);
780: }

782: static PetscErrorCode MatProductSetFromOptions_ConstDiag_Diagonal(Mat C)
783: {
784:   Mat_Product *product = C->product;

786:   PetscFunctionBegin;
787:   if (product->type == MATPRODUCT_PtAP) C->ops->productsymbolic = MatProductSymbolic_PtAP_ConstDiag_Diagonal;
788:   else if (product->type == MATPRODUCT_AB) C->ops->productsymbolic = MatProductSymbolic_AB_ConstDiag_Diagonal;
789:   PetscFunctionReturn(PETSC_SUCCESS);
790: }

792: static PetscErrorCode MatProductSetFromOptions_Diagonal_ConstDiag(Mat C)
793: {
794:   Mat_Product *product = C->product;

796:   PetscFunctionBegin;
797:   if (product->type == MATPRODUCT_PtAP) C->ops->productsymbolic = MatProductSymbolic_PtAP_Diagonal_ConstDiag;
798:   else if (product->type == MATPRODUCT_AB) C->ops->productsymbolic = MatProductSymbolic_AB_Diagonal_ConstDiag;
799:   PetscFunctionReturn(PETSC_SUCCESS);
800: }

802: static PetscErrorCode MatProductSetFromOptions_ConstDiag_Dense_AB(Mat C)
803: {
804:   PetscFunctionBegin;
805:   C->ops->productsymbolic = MatProductSymbolic_ConstDiag_Dense;
806:   PetscFunctionReturn(PETSC_SUCCESS);
807: }

809: static PetscErrorCode MatProductSetFromOptions_ConstDiag_Dense(Mat C)
810: {
811:   Mat_Product *product = C->product;

813:   PetscFunctionBegin;
814:   if (product->type == MATPRODUCT_AB || product->type == MATPRODUCT_AtB) PetscCall(MatProductSetFromOptions_ConstDiag_Dense_AB(C));
815:   else if (product->type == MATPRODUCT_PtAP) C->ops->productsymbolic = MatProductSymbolic_PtAP_ConstDiag_Anytype;
816:   PetscFunctionReturn(PETSC_SUCCESS);
817: }

819: static PetscErrorCode MatProductSetFromOptions_ConstDiag_Anytype(Mat C)
820: {
821:   Mat_Product *product = C->product;
822:   PetscBool    Acdiag, Bcdiag;

824:   PetscFunctionBegin;
825:   PetscCall(PetscObjectTypeCompare((PetscObject)product->A, MATCONSTANTDIAGONAL, &Acdiag));
826:   PetscCall(PetscObjectTypeCompare((PetscObject)product->B, MATCONSTANTDIAGONAL, &Bcdiag));
827:   if (Acdiag && !Bcdiag && (product->type == MATPRODUCT_PtAP)) C->ops->productsymbolic = MatProductSymbolic_PtAP_ConstDiag_Anytype;
828:   else if (Bcdiag && !Acdiag && (product->type == MATPRODUCT_PtAP)) C->ops->productsymbolic = MatProductSymbolic_PtAP_Anytype_ConstDiag;
829:   else if (Acdiag && !Bcdiag && (product->type == MATPRODUCT_AB)) C->ops->productsymbolic = MatProductSymbolic_AB_ConstDiag_Anytype;
830:   else if (Bcdiag && !Acdiag && (product->type == MATPRODUCT_AB)) C->ops->productsymbolic = MatProductSymbolic_AB_Anytype_ConstDiag;
831:   PetscFunctionReturn(PETSC_SUCCESS);
832: }

834: /*MC
835:    MATCONSTANTDIAGONAL - "constant-diagonal" - A diagonal matrix type with a uniform value
836:    along the diagonal.

838:   Level: advanced

840: .seealso: [](ch_matrices), `Mat`, `MatCreateConstantDiagonal()`
841: M*/
842: PETSC_EXTERN PetscErrorCode MatCreate_ConstantDiagonal(Mat A)
843: {
844:   Mat_ConstantDiagonal *ctx;

846:   PetscFunctionBegin;
847:   PetscCall(PetscNew(&ctx));
848:   ctx->diag = 0.0;
849:   A->data   = (void *)ctx;

851:   A->assembled                   = PETSC_TRUE;
852:   A->preallocated                = PETSC_TRUE;
853:   A->structurally_symmetric      = PETSC_BOOL3_TRUE;
854:   A->structural_symmetry_eternal = PETSC_TRUE;
855:   A->symmetric                   = PETSC_BOOL3_TRUE;
856:   if (!PetscDefined(USE_COMPLEX)) A->hermitian = PETSC_BOOL3_TRUE;
857:   A->symmetry_eternal = PETSC_TRUE;

859:   A->ops->mult                      = MatMult_ConstantDiagonal;
860:   A->ops->multadd                   = MatMultAdd_ConstantDiagonal;
861:   A->ops->multtranspose             = MatMult_ConstantDiagonal;
862:   A->ops->multtransposeadd          = MatMultAdd_ConstantDiagonal;
863:   A->ops->multhermitiantranspose    = MatMultHermitianTranspose_ConstantDiagonal;
864:   A->ops->multhermitiantransposeadd = MatMultHermitianTransposeAdd_ConstantDiagonal;
865:   A->ops->solve                     = MatSolve_ConstantDiagonal;
866:   A->ops->solvetranspose            = MatSolve_ConstantDiagonal;
867:   A->ops->norm                      = MatNorm_ConstantDiagonal;
868:   A->ops->createsubmatrices         = MatCreateSubMatrices_ConstantDiagonal;
869:   A->ops->duplicate                 = MatDuplicate_ConstantDiagonal;
870:   A->ops->getrow                    = MatGetRow_ConstantDiagonal;
871:   A->ops->restorerow                = MatRestoreRow_ConstantDiagonal;
872:   A->ops->sor                       = MatSOR_ConstantDiagonal;
873:   A->ops->shift                     = MatShift_ConstantDiagonal;
874:   A->ops->scale                     = MatScale_ConstantDiagonal;
875:   A->ops->getdiagonal               = MatGetDiagonal_ConstantDiagonal;
876:   A->ops->view                      = MatView_ConstantDiagonal;
877:   A->ops->zeroentries               = MatZeroEntries_ConstantDiagonal;
878:   A->ops->destroy                   = MatDestroy_ConstantDiagonal;
879:   A->ops->getinfo                   = MatGetInfo_ConstantDiagonal;
880:   A->ops->equal                     = MatEqual_ConstantDiagonal;
881:   A->ops->axpy                      = MatAXPY_ConstantDiagonal;
882:   A->ops->setrandom                 = MatSetRandom_ConstantDiagonal;
883:   A->ops->conjugate                 = MatConjugate_ConstantDiagonal;
884:   A->ops->transpose                 = MatTranspose_ConstantDiagonal;

886:   PetscCall(PetscObjectChangeTypeName((PetscObject)A, MATCONSTANTDIAGONAL));
887:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatConstantDiagonalGetConstant_C", MatConstantDiagonalGetConstant_ConstantDiagonal));
888:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_constantdiagonal_constantdiagonal_C", MatProductSetFromOptions_ConstDiag_ConstDiag));
889:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_constantdiagonal_diagonal_C", MatProductSetFromOptions_ConstDiag_Diagonal));
890:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_diagonal_constantdiagonal_C", MatProductSetFromOptions_Diagonal_ConstDiag));
891:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_constantdiagonal_seqdense_C", MatProductSetFromOptions_ConstDiag_Dense));
892:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_constantdiagonal_mpidense_C", MatProductSetFromOptions_ConstDiag_Dense));
893: #if PetscDefined(HAVE_CUDA)
894:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_constantdiagonal_seqdensecuda_C", MatProductSetFromOptions_ConstDiag_Dense));
895:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_constantdiagonal_mpidensecuda_C", MatProductSetFromOptions_ConstDiag_Dense));
896: #endif
897: #if PetscDefined(HAVE_HIP)
898:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_constantdiagonal_seqdensehip_C", MatProductSetFromOptions_ConstDiag_Dense));
899:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_constantdiagonal_mpidensehip_C", MatProductSetFromOptions_ConstDiag_Dense));
900: #endif
901:   PetscCall(PetscObjectComposeFunction((PetscObject)A, "MatProductSetFromOptions_anytype_C", MatProductSetFromOptions_ConstDiag_Anytype));
902:   PetscFunctionReturn(PETSC_SUCCESS);
903: }

905: static PetscErrorCode MatFactorNumeric_ConstantDiagonal(Mat fact, Mat A, const MatFactorInfo *info)
906: {
907:   Mat_ConstantDiagonal *actx = (Mat_ConstantDiagonal *)A->data, *fctx = (Mat_ConstantDiagonal *)fact->data;

909:   PetscFunctionBegin;
910:   if (actx->diag == 0.0) fact->factorerrortype = MAT_FACTOR_NUMERIC_ZEROPIVOT;
911:   else fact->factorerrortype = MAT_FACTOR_NOERROR;
912:   fctx->diag       = 1.0 / actx->diag;
913:   fact->ops->solve = MatMult_ConstantDiagonal;
914:   PetscFunctionReturn(PETSC_SUCCESS);
915: }

917: static PetscErrorCode MatFactorSymbolic_LU_ConstantDiagonal(Mat fact, Mat A, IS isrow, IS iscol, const MatFactorInfo *info)
918: {
919:   PetscFunctionBegin;
920:   fact->ops->lufactornumeric = MatFactorNumeric_ConstantDiagonal;
921:   PetscFunctionReturn(PETSC_SUCCESS);
922: }

924: static PetscErrorCode MatFactorSymbolic_Cholesky_ConstantDiagonal(Mat fact, Mat A, IS isrow, const MatFactorInfo *info)
925: {
926:   PetscFunctionBegin;
927:   fact->ops->choleskyfactornumeric = MatFactorNumeric_ConstantDiagonal;
928:   PetscFunctionReturn(PETSC_SUCCESS);
929: }

931: PETSC_INTERN PetscErrorCode MatGetFactor_constantdiagonal_petsc(Mat A, MatFactorType ftype, Mat *B)
932: {
933:   PetscInt n = A->rmap->n, N = A->rmap->N;

935:   PetscFunctionBegin;
936:   PetscCall(MatCreateConstantDiagonal(PetscObjectComm((PetscObject)A), n, n, N, N, 0, B));

938:   (*B)->factortype                  = ftype;
939:   (*B)->ops->ilufactorsymbolic      = MatFactorSymbolic_LU_ConstantDiagonal;
940:   (*B)->ops->lufactorsymbolic       = MatFactorSymbolic_LU_ConstantDiagonal;
941:   (*B)->ops->iccfactorsymbolic      = MatFactorSymbolic_Cholesky_ConstantDiagonal;
942:   (*B)->ops->choleskyfactorsymbolic = MatFactorSymbolic_Cholesky_ConstantDiagonal;

944:   (*B)->ops->shift       = NULL;
945:   (*B)->ops->scale       = NULL;
946:   (*B)->ops->mult        = NULL;
947:   (*B)->ops->sor         = NULL;
948:   (*B)->ops->zeroentries = NULL;

950:   PetscCall(PetscFree((*B)->solvertype));
951:   PetscCall(PetscStrallocpy(MATSOLVERPETSC, &(*B)->solvertype));
952:   PetscFunctionReturn(PETSC_SUCCESS);
953: }