Reference documentation for deal.II version 9.6.0
\(\newcommand{\dealvcentcolon}{\mathrel{\mathop{:}}}\) \(\newcommand{\dealcoloneq}{\dealvcentcolon\mathrel{\mkern-1.2mu}=}\) \(\newcommand{\jump}[1]{\left[\!\left[ #1 \right]\!\right]}\) \(\newcommand{\average}[1]{\left\{\!\left\{ #1 \right\}\!\right\}}\)
Loading...
Searching...
No Matches
face_setup_internal.h
Go to the documentation of this file.
1// ------------------------------------------------------------------------
2//
3// SPDX-License-Identifier: LGPL-2.1-or-later
4// Copyright (C) 2018 - 2024 by the deal.II authors
5//
6// This file is part of the deal.II library.
7//
8// Part of the source code is dual licensed under Apache-2.0 WITH
9// LLVM-exception OR LGPL-2.1-or-later. Detailed license information
10// governing the source code and code contributions can be found in
11// LICENSE.md and CONTRIBUTING.md at the top level directory of deal.II.
12//
13// ------------------------------------------------------------------------
14
15
16#ifndef dealii_face_setup_internal_h
17#define dealii_face_setup_internal_h
18
19#include <deal.II/base/config.h>
20
21#include <deal.II/base/memory_consumption.h>
22
23#include <deal.II/distributed/tria_base.h>
24
25#include <deal.II/grid/tria.h>
26#include <deal.II/grid/tria_accessor.h>
27
28#include <deal.II/matrix_free/face_info.h>
29#include <deal.II/matrix_free/shape_info.h>
30#include <deal.II/matrix_free/task_info.h>
31
32#include <fstream>
33
34
35DEAL_II_NAMESPACE_OPEN
36
37
38namespace internal
39{
40 namespace MatrixFreeFunctions
41 {
57
58
59
68 template <int dim>
69 struct FaceSetup
70 {
71 FaceSetup();
72
79 void
80 initialize(
81 const ::Triangulation<dim> &triangulation,
82 const unsigned int mg_level,
83 const bool hold_all_faces_to_owned_cells,
84 const bool build_inner_faces,
85 std::vector<std::pair<unsigned int, unsigned int>> &cell_levels);
86
93 void
94 generate_faces(
95 const ::Triangulation<dim> &triangulation,
96 const std::vector<std::pair<unsigned int, unsigned int>> &cell_levels,
97 TaskInfo &task_info);
98
105 FaceToCellTopology<1>
106 create_face(
107 const unsigned int face_no,
108 const typename ::Triangulation<dim>::cell_iterator &cell,
109 const unsigned int number_cell_interior,
110 const typename ::Triangulation<dim>::cell_iterator &neighbor,
111 const unsigned int number_cell_exterior,
112 const bool is_mixed_mesh);
113
114 bool use_active_cells;
115
128
129 std::vector<FaceCategory> face_is_owned;
130 std::vector<bool> at_processor_boundary;
131 std::vector<FaceToCellTopology<1>> inner_faces;
132 std::vector<FaceToCellTopology<1>> boundary_faces;
133 std::vector<FaceToCellTopology<1>> inner_ghost_faces;
134 std::vector<FaceToCellTopology<1>> refinement_edge_faces;
135 };
136
137
138
142 template <int vectorization_width>
143 void
144 collect_faces_vectorization(
145 const std::vector<FaceToCellTopology<1>> &faces_in,
146 const std::vector<bool> &hard_vectorization_boundary,
147 std::vector<unsigned int> &face_partition_data,
148 std::vector<FaceToCellTopology<vectorization_width>> &faces_out);
149
150
151
152 /* -------------------------------------------------------------------- */
153
154#ifndef DOXYGEN
155
156 template <int dim>
157 FaceSetup<dim>::FaceSetup()
158 : use_active_cells(true)
159 {}
160
161
162
163 template <int dim>
164 void
165 FaceSetup<dim>::initialize(
166 const ::Triangulation<dim> &triangulation,
167 const unsigned int mg_level,
168 const bool hold_all_faces_to_owned_cells,
169 const bool build_inner_faces,
170 std::vector<std::pair<unsigned int, unsigned int>> &cell_levels)
171 {
172 use_active_cells = mg_level == numbers::invalid_unsigned_int;
173
174# ifdef DEBUG
175 // safety check
176 if (use_active_cells)
177 for (const auto &cell_level : cell_levels)
178 {
179 typename ::Triangulation<dim>::cell_iterator dcell(
180 &triangulation, cell_level.first, cell_level.second);
181 Assert(dcell->is_active(), ExcInternalError());
182 }
183# endif
184
185 // step 1: add ghost cells for those cells that we identify as
186 // interesting
187
188 at_processor_boundary.resize(cell_levels.size(), false);
189 face_is_owned.resize(dim > 1 ? triangulation.n_raw_faces() :
190 triangulation.n_vertices(),
191 FaceCategory::locally_active_done_elsewhere);
192
193 // go through the mesh and divide the faces on the processor
194 // boundaries as evenly as possible between the processors
195 std::map<types::subdomain_id, FaceIdentifier>
196 inner_faces_at_proc_boundary;
197 if (triangulation.locally_owned_subdomain() !=
198 numbers::invalid_subdomain_id)
199 {
200 const types::subdomain_id my_domain =
201 triangulation.locally_owned_subdomain();
202 for (unsigned int i = 0; i < cell_levels.size(); ++i)
203 {
204 if (i > 0 && cell_levels[i] == cell_levels[i - 1])
205 continue;
206 typename ::Triangulation<dim>::cell_iterator dcell(
207 &triangulation, cell_levels[i].first, cell_levels[i].second);
208 for (const unsigned int f : dcell->face_indices())
209 {
210 if (dcell->at_boundary(f) && !dcell->has_periodic_neighbor(f))
211 continue;
212 typename ::Triangulation<dim>::cell_iterator neighbor =
213 dcell->neighbor_or_periodic_neighbor(f);
214
215 // faces at hanging nodes are always treated by the processor
216 // who owns the element on the fine side. but we need to count
217 // the number of inner faces in order to balance the remaining
218 // faces properly
219 const CellId id_mine = dcell->id();
220 if (use_active_cells && neighbor->has_children())
221 for (unsigned int c = 0;
222 c < (dcell->has_periodic_neighbor(f) ?
223 dcell->periodic_neighbor(f)
224 ->face(dcell->periodic_neighbor_face_no(f))
225 ->n_children() :
226 dcell->face(f)->n_children());
227 ++c)
228 {
229 typename ::Triangulation<dim>::cell_iterator
230 neighbor_c =
231 dcell->at_boundary(f) ?
232 dcell->periodic_neighbor_child_on_subface(f, c) :
233 dcell->neighbor_child_on_subface(f, c);
234 const types::subdomain_id neigh_domain =
235 neighbor_c->subdomain_id();
236 if (my_domain < neigh_domain)
237 inner_faces_at_proc_boundary[neigh_domain]
238 .n_hanging_faces_larger_subdomain++;
239 else if (my_domain > neigh_domain)
240 inner_faces_at_proc_boundary[neigh_domain]
241 .n_hanging_faces_smaller_subdomain++;
242 }
243 else
244 {
245 const types::subdomain_id neigh_domain =
246 use_active_cells ? neighbor->subdomain_id() :
247 neighbor->level_subdomain_id();
248 if (neighbor->level() < dcell->level() &&
249 use_active_cells)
250 {
251 if (my_domain < neigh_domain)
252 inner_faces_at_proc_boundary[neigh_domain]
253 .n_hanging_faces_smaller_subdomain++;
254 else if (my_domain > neigh_domain)
255 inner_faces_at_proc_boundary[neigh_domain]
256 .n_hanging_faces_larger_subdomain++;
257 }
258 else if (neighbor->level() == dcell->level() &&
259 my_domain != neigh_domain)
260 {
261 // always list the cell whose owner has the lower
262 // subdomain id first. this applies to both processors
263 // involved, so both processors will generate the same
264 // list that we will later order
265 const CellId id_neigh = neighbor->id();
266 if (my_domain < neigh_domain)
267 inner_faces_at_proc_boundary[neigh_domain]
268 .shared_faces.emplace_back(id_mine, id_neigh);
269 else
270 inner_faces_at_proc_boundary[neigh_domain]
271 .shared_faces.emplace_back(id_neigh, id_mine);
272 }
273 }
274 }
275 }
276
277 // sort the cell ids related to each neighboring processor. This
278 // algorithm is symmetric so every processor combination should
279 // arrive here and no deadlock should be possible
280 for (auto &inner_face : inner_faces_at_proc_boundary)
281 {
282 Assert(inner_face.first != my_domain,
283 ExcInternalError("Should not send info to myself"));
284 std::sort(inner_face.second.shared_faces.begin(),
285 inner_face.second.shared_faces.end());
286 inner_face.second.shared_faces.erase(
287 std::unique(inner_face.second.shared_faces.begin(),
288 inner_face.second.shared_faces.end()),
289 inner_face.second.shared_faces.end());
290
291 // safety check: both involved processors should see the same list
292 // because the pattern of ghosting is symmetric. We test this by
293 // looking at the length of the lists of faces
294# if defined(DEAL_II_WITH_MPI) && defined(DEBUG)
295 MPI_Comm comm = MPI_COMM_SELF;
296 if (const ::parallel::TriangulationBase<dim> *ptria =
297 dynamic_cast<const ::parallel::TriangulationBase<dim>
298 *>(&triangulation))
299 comm = ptria->get_communicator();
300
301 MPI_Status status;
302 unsigned int mysize = inner_face.second.shared_faces.size();
303 unsigned int othersize = numbers::invalid_unsigned_int;
304
305 int ierr = MPI_Sendrecv(&mysize,
306 1,
307 MPI_UNSIGNED,
308 inner_face.first,
309 600 + my_domain,
310 &othersize,
311 1,
312 MPI_UNSIGNED,
313 inner_face.first,
314 600 + inner_face.first,
315 comm,
316 &status);
317 AssertThrowMPI(ierr);
318 AssertDimension(mysize, othersize);
319 mysize = inner_face.second.n_hanging_faces_smaller_subdomain;
320 ierr = MPI_Sendrecv(&mysize,
321 1,
322 MPI_UNSIGNED,
323 inner_face.first,
324 700 + my_domain,
325 &othersize,
326 1,
327 MPI_UNSIGNED,
328 inner_face.first,
329 700 + inner_face.first,
330 comm,
331 &status);
332 AssertThrowMPI(ierr);
333 AssertDimension(mysize, othersize);
334 mysize = inner_face.second.n_hanging_faces_larger_subdomain;
335 ierr = MPI_Sendrecv(&mysize,
336 1,
337 MPI_UNSIGNED,
338 inner_face.first,
339 800 + my_domain,
340 &othersize,
341 1,
342 MPI_UNSIGNED,
343 inner_face.first,
344 800 + inner_face.first,
345 comm,
346 &status);
347 AssertThrowMPI(ierr);
348 AssertDimension(mysize, othersize);
349# endif
350
351 // Arrange the face "ownership" such that cells that are access
352 // by more than one face (think of a cell in a corner) get
353 // ghosted. This arrangement has the advantage that we need to
354 // send less data because the same data is used twice. The
355 // strategy applied here is to ensure the same order of face
356 // pairs on both processors that share some faces, and make the
357 // same decision on both sides.
358
359 // Create a vector with cell ids sorted over the processor with
360 // the larger rank. In the code below we need to be able to
361 // identify the same cell once for the processor with higher
362 // rank and once for the processor with the lower rank. The
363 // format for the processor with the higher rank is already
364 // contained in `shared_faces`, whereas we need a copy that we
365 // sort differently for the other way around.
366 std::vector<std::tuple<CellId, CellId, unsigned int>> other_range(
367 inner_face.second.shared_faces.size());
368 for (unsigned int i = 0; i < other_range.size(); ++i)
369 other_range[i] =
370 std::make_tuple(inner_face.second.shared_faces[i].second,
371 inner_face.second.shared_faces[i].first,
372 i);
373 std::sort(other_range.begin(), other_range.end());
374
375 // the vector 'assignment' sets whether a particular cell
376 // appears more often and acts as a pre-selection of the rank. A
377 // value of 1 means that the process with the higher rank gets
378 // those faces, a value -1 means that the process with the lower
379 // rank gets it, whereas a value 0 means that the decision can
380 // be made in an arbitrary way.
381 unsigned int n_faces_lower_proc = 0, n_faces_higher_proc = 0;
382 std::vector<signed char> assignment(other_range.size(), 0);
383 if (inner_face.second.shared_faces.size() > 0)
384 {
385 // identify faces that go to the processor with the higher
386 // rank
387 unsigned int count = 0;
388 for (unsigned int i = 1;
389 i < inner_face.second.shared_faces.size();
390 ++i)
391 if (inner_face.second.shared_faces[i].first ==
392 inner_face.second.shared_faces[i - 1 - count].first)
393 ++count;
394 else
395 {
396 AssertThrow(count < 2 * dim, ExcInternalError());
397 if (count > 0)
398 {
399 for (unsigned int k = 0; k <= count; ++k)
400 assignment[i - 1 - k] = 1;
401 n_faces_higher_proc += count + 1;
402 }
403 count = 0;
404 }
405
406 // identify faces that definitely go to the processor with
407 // the lower rank - this must use the sorting of CellId
408 // variables from the processor with the higher rank, i.e.,
409 // other_range rather than `shared_faces`.
410 count = 0;
411 for (unsigned int i = 1; i < other_range.size(); ++i)
412 if (std::get<0>(other_range[i]) ==
413 std::get<0>(other_range[i - 1 - count]))
414 ++count;
415 else
416 {
417 AssertThrow(count < 2 * dim, ExcInternalError());
418 if (count > 0)
419 {
420 for (unsigned int k = 0; k <= count; ++k)
421 {
422 Assert(inner_face.second
423 .shared_faces[std::get<2>(
424 other_range[i - 1])]
425 .second ==
426 inner_face.second
427 .shared_faces[std::get<2>(
428 other_range[i - 1 - k])]
429 .second,
430 ExcInternalError());
431 // only assign to -1 if higher rank was not
432 // yet set
433 if (assignment[std::get<2>(
434 other_range[i - 1 - k])] == 0)
435 {
436 assignment[std::get<2>(
437 other_range[i - 1 - k])] = -1;
438 ++n_faces_lower_proc;
439 }
440 }
441 }
442 count = 0;
443 }
444 }
445
446
447 // divide the faces evenly between the two processors. the
448 // processor with small rank takes the first half, the processor
449 // with larger rank the second half. Adjust for the hanging
450 // faces that always get assigned to one side, and the faces we
451 // have already assigned due to the criterion above
452 n_faces_lower_proc +=
453 inner_face.second.n_hanging_faces_smaller_subdomain;
454 n_faces_higher_proc +=
455 inner_face.second.n_hanging_faces_larger_subdomain;
456 const unsigned int n_total_faces_at_proc_boundary =
457 (inner_face.second.shared_faces.size() +
458 inner_face.second.n_hanging_faces_smaller_subdomain +
459 inner_face.second.n_hanging_faces_larger_subdomain);
460 unsigned int split_index = n_total_faces_at_proc_boundary / 2;
461 if (split_index < n_faces_lower_proc)
462 split_index = 0;
463 else if (split_index <
464 n_total_faces_at_proc_boundary - n_faces_higher_proc)
465 split_index -= n_faces_lower_proc;
466 else
467 split_index = n_total_faces_at_proc_boundary -
468 n_faces_higher_proc - n_faces_lower_proc;
469
470 // make sure the splitting is consistent between both sides
471# if defined(DEAL_II_WITH_MPI) && defined(DEBUG)
472 ierr = MPI_Sendrecv(&split_index,
473 1,
474 MPI_UNSIGNED,
475 inner_face.first,
476 900 + my_domain,
477 &othersize,
478 1,
479 MPI_UNSIGNED,
480 inner_face.first,
481 900 + inner_face.first,
482 comm,
483 &status);
484 AssertThrowMPI(ierr);
485 AssertDimension(split_index, othersize);
486 ierr = MPI_Sendrecv(&n_faces_lower_proc,
487 1,
488 MPI_UNSIGNED,
489 inner_face.first,
490 1000 + my_domain,
491 &othersize,
492 1,
493 MPI_UNSIGNED,
494 inner_face.first,
495 1000 + inner_face.first,
496 comm,
497 &status);
498 AssertThrowMPI(ierr);
499 AssertDimension(n_faces_lower_proc, othersize);
500 ierr = MPI_Sendrecv(&n_faces_higher_proc,
501 1,
502 MPI_UNSIGNED,
503 inner_face.first,
504 1100 + my_domain,
505 &othersize,
506 1,
507 MPI_UNSIGNED,
508 inner_face.first,
509 1100 + inner_face.first,
510 comm,
511 &status);
512 AssertThrowMPI(ierr);
513 AssertDimension(n_faces_higher_proc, othersize);
514# endif
515
516 // collect the faces on both sides
517 std::vector<std::pair<CellId, CellId>> owned_faces_lower,
518 owned_faces_higher;
519 for (unsigned int i = 0; i < assignment.size(); ++i)
520 if (assignment[i] < 0)
521 owned_faces_lower.push_back(
522 inner_face.second.shared_faces[i]);
523 else if (assignment[i] > 0)
524 owned_faces_higher.push_back(
525 inner_face.second.shared_faces[i]);
526 AssertIndexRange(split_index,
527 inner_face.second.shared_faces.size() + 1 -
528 owned_faces_lower.size() -
529 owned_faces_higher.size());
530
531 unsigned int i = 0, c = 0;
532 for (; i < assignment.size() && c < split_index; ++i)
533 if (assignment[i] == 0)
534 {
535 owned_faces_lower.push_back(
536 inner_face.second.shared_faces[i]);
537 ++c;
538 }
539 for (; i < assignment.size(); ++i)
540 if (assignment[i] == 0)
541 {
542 owned_faces_higher.push_back(
543 inner_face.second.shared_faces[i]);
544 }
545
546# ifdef DEBUG
547 // check consistency of faces on both sides
548 std::vector<std::pair<CellId, CellId>> check_faces;
549 check_faces.insert(check_faces.end(),
550 owned_faces_lower.begin(),
551 owned_faces_lower.end());
552 check_faces.insert(check_faces.end(),
553 owned_faces_higher.begin(),
554 owned_faces_higher.end());
555 std::sort(check_faces.begin(), check_faces.end());
556 AssertDimension(check_faces.size(),
557 inner_face.second.shared_faces.size());
558 for (unsigned int i = 0; i < check_faces.size(); ++i)
559 Assert(check_faces[i] == inner_face.second.shared_faces[i],
560 ExcInternalError());
561# endif
562
563 // now only set half of the faces as the ones to keep
564 if (my_domain < inner_face.first)
565 inner_face.second.shared_faces.swap(owned_faces_lower);
566 else
567 inner_face.second.shared_faces.swap(owned_faces_higher);
568
569 std::sort(inner_face.second.shared_faces.begin(),
570 inner_face.second.shared_faces.end());
571 }
572 }
573
574 // fill in the additional cells that we need access to via ghosting to
575 // cell_levels
576 std::set<std::pair<unsigned int, unsigned int>> ghost_cells;
577 for (unsigned int i = 0; i < cell_levels.size(); ++i)
578 {
579 typename ::Triangulation<dim>::cell_iterator dcell(
580 &triangulation, cell_levels[i].first, cell_levels[i].second);
581 if (use_active_cells)
582 Assert(dcell->is_active(), ExcNotImplemented());
583 for (const auto f : dcell->face_indices())
584 {
585 if (dcell->at_boundary(f) && !dcell->has_periodic_neighbor(f))
586 face_is_owned[dcell->face(f)->index()] =
587 FaceCategory::locally_active_at_boundary;
588 else if (!build_inner_faces)
589 continue;
590
591 // treat boundaries of cells of different refinement level
592 // inside the domain in case of multigrid separately
593 else if ((dcell->at_boundary(f) == false ||
594 dcell->has_periodic_neighbor(f)) &&
595 mg_level != numbers::invalid_unsigned_int &&
596 dcell->neighbor_or_periodic_neighbor(f)->level() <
597 dcell->level())
598 {
599 face_is_owned[dcell->face(f)->index()] =
600 FaceCategory::multigrid_refinement_edge;
601 }
602 else
603 {
604 typename ::Triangulation<dim>::cell_iterator neighbor =
605 dcell->neighbor_or_periodic_neighbor(f);
606
607 // neighbor is refined -> face will be treated by neighbor
608 if (use_active_cells && neighbor->has_children() &&
609 hold_all_faces_to_owned_cells == false)
610 continue;
611
612 bool add_to_ghost = false;
613 const types::subdomain_id
614 id1 = use_active_cells ? dcell->subdomain_id() :
615 dcell->level_subdomain_id(),
616 id2 = use_active_cells ?
617 (neighbor->has_children() ?
618 dcell->neighbor_child_on_subface(f, 0)
619 ->subdomain_id() :
620 neighbor->subdomain_id()) :
621 neighbor->level_subdomain_id();
622
623 // Check whether the current face should be processed
624 // locally (instead of being processed from the other
625 // side). We process a face locally when we are more refined
626 // (in the active cell case) or when the face is listed in
627 // the `shared_faces` data structure that we built above.
628 if ((id1 == id2 &&
629 (use_active_cells == false || neighbor->is_active())) ||
630 dcell->level() > neighbor->level() ||
631 std::binary_search(
632 inner_faces_at_proc_boundary[id2].shared_faces.begin(),
633 inner_faces_at_proc_boundary[id2].shared_faces.end(),
634 std::make_pair(id1 < id2 ? dcell->id() : neighbor->id(),
635 id1 < id2 ? neighbor->id() :
636 dcell->id())))
637 {
638 face_is_owned[dcell->face(f)->index()] =
639 FaceCategory::locally_active_done_here;
640 if (dcell->level() == neighbor->level())
641 face_is_owned
642 [neighbor
643 ->face(dcell->has_periodic_neighbor(f) ?
644 dcell->periodic_neighbor_face_no(f) :
645 dcell->neighbor_face_no(f))
646 ->index()] =
647 FaceCategory::locally_active_done_here;
648
649 // If neighbor is a ghost element (i.e.
650 // dcell->subdomain_id !
651 // dcell->neighbor(f)->subdomain_id()), we need to add its
652 // index into cell level list.
653 if (use_active_cells)
654 add_to_ghost =
655 (dcell->subdomain_id() != neighbor->subdomain_id());
656 else
657 add_to_ghost = (dcell->level_subdomain_id() !=
658 neighbor->level_subdomain_id());
659 }
660 else if (hold_all_faces_to_owned_cells == true)
661 {
662 // add all cells to ghost layer...
663 face_is_owned[dcell->face(f)->index()] =
664 FaceCategory::ghosted;
665 if (use_active_cells)
666 {
667 if (neighbor->has_children())
668 for (unsigned int s = 0;
669 s < dcell->face(f)->n_children();
670 ++s)
671 if (dcell->at_boundary(f))
672 {
673 if (dcell
674 ->periodic_neighbor_child_on_subface(f,
675 s)
676 ->subdomain_id() !=
677 dcell->subdomain_id())
678 add_to_ghost = true;
679 }
680 else
681 {
682 if (dcell->neighbor_child_on_subface(f, s)
683 ->subdomain_id() !=
684 dcell->subdomain_id())
685 add_to_ghost = true;
686 }
687 else
688 add_to_ghost = (dcell->subdomain_id() !=
689 neighbor->subdomain_id());
690 }
691 else
692 add_to_ghost = (dcell->level_subdomain_id() !=
693 neighbor->level_subdomain_id());
694 }
695
696 if (add_to_ghost)
697 {
698 if (use_active_cells && neighbor->has_children())
699 for (unsigned int s = 0;
700 s < dcell->face(f)->n_children();
701 ++s)
702 {
703 typename ::Triangulation<dim>::cell_iterator
704 neighbor_child =
705 dcell->at_boundary(f) ?
706 dcell->periodic_neighbor_child_on_subface(f,
707 s) :
708 dcell->neighbor_child_on_subface(f, s);
709 if (neighbor_child->subdomain_id() !=
710 dcell->subdomain_id())
711 ghost_cells.insert(
712 std::pair<unsigned int, unsigned int>(
713 neighbor_child->level(),
714 neighbor_child->index()));
715 }
716 else
717 ghost_cells.insert(
718 std::pair<unsigned int, unsigned int>(
719 neighbor->level(), neighbor->index()));
720 at_processor_boundary[i] = true;
721 }
722 }
723 }
724 }
725
726 // step 2: append the ghost cells at the end of the locally owned
727 // cells
728 for (const auto &ghost_cell : ghost_cells)
729 cell_levels.push_back(ghost_cell);
730 }
731
732
733
734 template <int dim>
735 void
736 FaceSetup<dim>::generate_faces(
737 const ::Triangulation<dim> &triangulation,
738 const std::vector<std::pair<unsigned int, unsigned int>> &cell_levels,
739 TaskInfo &task_info)
740 {
741 const bool is_mixed_mesh = triangulation.is_mixed_mesh();
742
743 // step 1: create the inverse map between cell iterators and the
744 // cell_level_index field
745 std::map<std::pair<unsigned int, unsigned int>, unsigned int>
746 map_to_vectorized;
747 for (unsigned int cell = 0; cell < cell_levels.size(); ++cell)
748 if (cell == 0 || cell_levels[cell] != cell_levels[cell - 1])
749 {
750 typename ::Triangulation<dim>::cell_iterator dcell(
751 &triangulation,
752 cell_levels[cell].first,
753 cell_levels[cell].second);
754 std::pair<unsigned int, unsigned int> level_index(dcell->level(),
755 dcell->index());
756 map_to_vectorized[level_index] = cell;
757 }
758
759 // step 2: fill the information about inner faces and boundary faces
760 const unsigned int vectorization_length = task_info.vectorization_length;
761 task_info.face_partition_data.resize(
762 task_info.cell_partition_data.size() - 1, 0);
763 task_info.boundary_partition_data.resize(
764 task_info.cell_partition_data.size() - 1, 0);
765 std::vector<unsigned char> face_visited(face_is_owned.size(), 0);
766 for (unsigned int partition = 0;
767 partition < task_info.cell_partition_data.size() - 2;
768 ++partition)
769 {
770 unsigned int boundary_counter = 0;
771 unsigned int inner_counter = 0;
772 for (unsigned int cell = task_info.cell_partition_data[partition] *
773 vectorization_length;
774 cell < task_info.cell_partition_data[partition + 1] *
775 vectorization_length;
776 ++cell)
777 if (cell == 0 || cell_levels[cell] != cell_levels[cell - 1])
778 {
779 typename ::Triangulation<dim>::cell_iterator dcell(
780 &triangulation,
781 cell_levels[cell].first,
782 cell_levels[cell].second);
783 for (const auto f : dcell->face_indices())
784 {
785 // boundary face
786 if (face_is_owned[dcell->face(f)->index()] ==
787 FaceCategory::locally_active_at_boundary)
788 {
789 Assert(dcell->at_boundary(f), ExcInternalError());
790 ++boundary_counter;
791 FaceToCellTopology<1> info;
792 info.cells_interior[0] = cell;
793 info.cells_exterior[0] = numbers::invalid_unsigned_int;
794 info.interior_face_no = f;
795 info.exterior_face_no = dcell->face(f)->boundary_id();
796 info.face_type =
797 is_mixed_mesh ?
798 (dcell->face(f)->reference_cell() !=
799 ReferenceCells::get_hypercube<dim - 1>()) :
800 0;
801 info.subface_index =
802 GeometryInfo<dim>::max_children_per_cell;
803 info.face_orientation = 0;
804 boundary_faces.push_back(info);
805
806 face_visited[dcell->face(f)->index()]++;
807 }
808 // interior face, including faces over periodic boundaries
809 else
810 {
811 typename ::Triangulation<dim>::cell_iterator
812 neighbor = dcell->neighbor_or_periodic_neighbor(f);
813 if (use_active_cells && neighbor->has_children())
814 {
815 for (unsigned int c = 0;
816 c < dcell->face(f)->n_children();
817 ++c)
818 {
819 typename ::Triangulation<
820 dim>::cell_iterator neighbor_c =
821 dcell->at_boundary(f) ?
822 dcell->periodic_neighbor_child_on_subface(
823 f, c) :
824 dcell->neighbor_child_on_subface(f, c);
825 const types::subdomain_id neigh_domain =
826 neighbor_c->subdomain_id();
827 const unsigned int neighbor_face_no =
828 dcell->has_periodic_neighbor(f) ?
829 dcell->periodic_neighbor_face_no(f) :
830 dcell->neighbor_face_no(f);
831 if (neigh_domain != dcell->subdomain_id() ||
832 face_visited
833 [dcell->face(f)->child(c)->index()] ==
834 1)
835 {
836 std::pair<unsigned int, unsigned int>
837 level_index(neighbor_c->level(),
838 neighbor_c->index());
839 if (face_is_owned
840 [dcell->face(f)->child(c)->index()] ==
841 FaceCategory::locally_active_done_here)
842 {
843 ++inner_counter;
844 inner_faces.push_back(create_face(
845 neighbor_face_no,
846 neighbor_c,
847 map_to_vectorized[level_index],
848 dcell,
849 cell,
850 is_mixed_mesh));
851 }
852 else if (face_is_owned[dcell->face(f)
853 ->child(c)
854 ->index()] ==
855 FaceCategory::ghosted)
856 {
857 inner_ghost_faces.push_back(create_face(
858 neighbor_face_no,
859 neighbor_c,
860 map_to_vectorized[level_index],
861 dcell,
862 cell,
863 is_mixed_mesh));
864 }
865 else
866 Assert(
867 face_is_owned[dcell->face(f)
868 ->index()] ==
869 FaceCategory::
870 locally_active_done_elsewhere ||
871 face_is_owned[dcell->face(f)
872 ->index()] ==
873 FaceCategory::ghosted,
874 ExcInternalError());
875 }
876 else
877 {
878 face_visited
879 [dcell->face(f)->child(c)->index()] = 1;
880 }
881 }
882 }
883 else
884 {
885 const types::subdomain_id my_domain =
886 use_active_cells ? dcell->subdomain_id() :
887 dcell->level_subdomain_id();
888 const types::subdomain_id neigh_domain =
889 use_active_cells ? neighbor->subdomain_id() :
890 neighbor->level_subdomain_id();
891 if (neigh_domain != my_domain ||
892 face_visited[dcell->face(f)->index()] == 1)
893 {
894 std::pair<unsigned int, unsigned int>
895 level_index(neighbor->level(),
896 neighbor->index());
897 if (face_is_owned[dcell->face(f)->index()] ==
898 FaceCategory::locally_active_done_here)
899 {
900 Assert(use_active_cells ||
901 dcell->level() ==
902 neighbor->level(),
903 ExcInternalError());
904 ++inner_counter;
905 inner_faces.push_back(create_face(
906 f,
907 dcell,
908 cell,
909 neighbor,
910 map_to_vectorized[level_index],
911 is_mixed_mesh));
912 }
913 else if (face_is_owned[dcell->face(f)
914 ->index()] ==
915 FaceCategory::ghosted)
916 {
917 inner_ghost_faces.push_back(create_face(
918 f,
919 dcell,
920 cell,
921 neighbor,
922 map_to_vectorized[level_index],
923 is_mixed_mesh));
924 }
925 }
926 else
927 {
928 face_visited[dcell->face(f)->index()] = 1;
929 if (dcell->has_periodic_neighbor(f))
930 face_visited
931 [neighbor
932 ->face(
933 dcell->periodic_neighbor_face_no(f))
934 ->index()] = 1;
935 }
936 if (face_is_owned[dcell->face(f)->index()] ==
937 FaceCategory::multigrid_refinement_edge)
938 {
939 refinement_edge_faces.push_back(
940 create_face(f,
941 dcell,
942 cell,
943 neighbor,
944 refinement_edge_faces.size(),
945 is_mixed_mesh));
946 }
947 }
948 }
949 }
950 }
951 task_info.face_partition_data[partition + 1] =
952 task_info.face_partition_data[partition] + inner_counter;
953 task_info.boundary_partition_data[partition + 1] =
954 task_info.boundary_partition_data[partition] + boundary_counter;
955 }
956 task_info.ghost_face_partition_data.resize(2);
957 task_info.ghost_face_partition_data[0] = 0;
958 task_info.ghost_face_partition_data[1] = inner_ghost_faces.size();
959 task_info.refinement_edge_face_partition_data.resize(2);
960 task_info.refinement_edge_face_partition_data[0] = 0;
961 task_info.refinement_edge_face_partition_data[1] =
962 refinement_edge_faces.size();
963 }
964
965
966
967 template <int dim>
968 FaceToCellTopology<1>
969 FaceSetup<dim>::create_face(
970 const unsigned int face_no,
971 const typename ::Triangulation<dim>::cell_iterator &cell,
972 const unsigned int number_cell_interior,
973 const typename ::Triangulation<dim>::cell_iterator &neighbor,
974 const unsigned int number_cell_exterior,
975 const bool is_mixed_mesh)
976 {
977 FaceToCellTopology<1> info;
978 info.cells_interior[0] = number_cell_interior;
979 info.cells_exterior[0] = number_cell_exterior;
980 info.interior_face_no = face_no;
981 if (cell->has_periodic_neighbor(face_no))
982 info.exterior_face_no = cell->periodic_neighbor_face_no(face_no);
983 else
984 info.exterior_face_no = cell->neighbor_face_no(face_no);
985
986 info.face_type = is_mixed_mesh ?
987 (cell->face(face_no)->reference_cell() !=
988 ReferenceCells::get_hypercube<dim - 1>()) :
989 0;
990
991 info.subface_index = GeometryInfo<dim>::max_children_per_cell;
992 Assert(neighbor->level() <= cell->level(), ExcInternalError());
993 if (cell->level() > neighbor->level())
994 {
995 if (cell->has_periodic_neighbor(face_no))
996 info.subface_index =
997 cell->periodic_neighbor_of_coarser_periodic_neighbor(face_no)
998 .second;
999 else
1000 info.subface_index =
1001 cell->neighbor_of_coarser_neighbor(face_no).second;
1002 }
1003
1004 // special treatment of periodic boundaries
1005 if (dim == 3 && cell->has_periodic_neighbor(face_no))
1006 {
1007 unsigned char exterior_face_orientation = cell->get_triangulation()
1008 .get_periodic_face_map()
1009 .at({cell, face_no})
1010 .second;
1011 const auto [orientation, rotation, flip] =
1012 ::internal::split_face_orientation(
1013 exterior_face_orientation);
1014
1015 info.face_orientation =
1016 (orientation ? 0u : 1u) + 2 * flip + 4 * rotation;
1017
1018 return info;
1019 }
1020
1021 info.face_orientation = 0;
1022 const unsigned int interior_face_orientation =
1023 !cell->face_orientation(face_no) + 2 * cell->face_flip(face_no) +
1024 4 * cell->face_rotation(face_no);
1025 const unsigned int exterior_face_orientation =
1026 !neighbor->face_orientation(info.exterior_face_no) +
1027 2 * neighbor->face_flip(info.exterior_face_no) +
1028 4 * neighbor->face_rotation(info.exterior_face_no);
1029 if (interior_face_orientation != 0)
1030 {
1031 info.face_orientation = 8 + interior_face_orientation;
1032 Assert(exterior_face_orientation == 0,
1033 ExcMessage(
1034 "Face seems to be wrongly oriented from both sides"));
1035 }
1036 else
1037 info.face_orientation = exterior_face_orientation;
1038
1039 // make sure to select correct subface index in case of non-standard
1040 // orientation of the coarser neighbor face
1041 if (cell->level() > neighbor->level() && exterior_face_orientation > 0)
1042 {
1043 const Table<2, unsigned int> orientation =
1044 ShapeInfo<double>::compute_orientation_table(2);
1045 const std::array<unsigned int, 8> inverted_orientations{
1046 {0, 1, 2, 3, 6, 5, 4, 7}};
1047 info.subface_index =
1048 orientation[inverted_orientations[exterior_face_orientation]]
1049 [info.subface_index];
1050 }
1051
1052 return info;
1053 }
1054
1055
1056
1063 inline bool
1064 compare_faces_for_vectorization(
1065 const FaceToCellTopology<1> &face1,
1066 const FaceToCellTopology<1> &face2,
1067 const std::vector<unsigned int> &active_fe_indices,
1068 const unsigned int length)
1069 {
1070 if (face1.interior_face_no != face2.interior_face_no)
1071 return false;
1072 if (face1.exterior_face_no != face2.exterior_face_no)
1073 return false;
1074 if (face1.subface_index != face2.subface_index)
1075 return false;
1076 if (face1.face_orientation != face2.face_orientation)
1077 return false;
1078 if (face1.face_type != face2.face_type)
1079 return false;
1080
1081 if (active_fe_indices.size() > 0)
1082 {
1083 if (active_fe_indices[face1.cells_interior[0] / length] !=
1084 active_fe_indices[face2.cells_interior[0] / length])
1085 return false;
1086
1087 if (face2.cells_exterior[0] != numbers::invalid_unsigned_int)
1088 if (active_fe_indices[face1.cells_exterior[0] / length] !=
1089 active_fe_indices[face2.cells_exterior[0] / length])
1090 return false;
1091 }
1092
1093 return true;
1094 }
1095
1096
1097
1104 template <int length>
1105 struct FaceComparator
1106 {
1107 FaceComparator(const std::vector<unsigned int> &active_fe_indices)
1108 : active_fe_indices(active_fe_indices)
1109 {}
1110
1111 bool
1112 operator()(const FaceToCellTopology<length> &face1,
1113 const FaceToCellTopology<length> &face2) const
1114 {
1115 // check if active FE indices match
1116 if (face1.face_type < face2.face_type)
1117 return true;
1118 else if (face1.face_type > face2.face_type)
1119 return false;
1120
1121 // check if active FE indices match
1122 if (active_fe_indices.size() > 0)
1123 {
1124 // ... for interior faces
1125 if (active_fe_indices[face1.cells_interior[0] / length] <
1126 active_fe_indices[face2.cells_interior[0] / length])
1127 return true;
1128 else if (active_fe_indices[face1.cells_interior[0] / length] >
1129 active_fe_indices[face2.cells_interior[0] / length])
1130 return false;
1131
1132 // ... for exterior faces
1133 if (face2.cells_exterior[0] != numbers::invalid_unsigned_int)
1134 {
1135 if (active_fe_indices[face1.cells_exterior[0] / length] <
1136 active_fe_indices[face2.cells_exterior[0] / length])
1137 return true;
1138 else if (active_fe_indices[face1.cells_exterior[0] / length] >
1139 active_fe_indices[face2.cells_exterior[0] / length])
1140 return false;
1141 }
1142 }
1143
1144 for (unsigned int i = 0; i < length; ++i)
1145 if (face1.cells_interior[i] < face2.cells_interior[i])
1146 return true;
1147 else if (face1.cells_interior[i] > face2.cells_interior[i])
1148 return false;
1149 for (unsigned int i = 0; i < length; ++i)
1150 if (face1.cells_exterior[i] < face2.cells_exterior[i])
1151 return true;
1152 else if (face1.cells_exterior[i] > face2.cells_exterior[i])
1153 return false;
1154 if (face1.interior_face_no < face2.interior_face_no)
1155 return true;
1156 else if (face1.interior_face_no > face2.interior_face_no)
1157 return false;
1158 if (face1.exterior_face_no < face2.exterior_face_no)
1159 return true;
1160 else if (face1.exterior_face_no > face2.exterior_face_no)
1161 return false;
1162
1163 // we do not need to check for subface_index and orientation because
1164 // those cannot be different if when all the other values are the
1165 // same.
1166 AssertDimension(face1.subface_index, face2.subface_index);
1167 AssertDimension(face1.face_orientation, face2.face_orientation);
1168
1169 return false;
1170 }
1171
1172 private:
1173 const std::vector<unsigned int> &active_fe_indices;
1174 };
1175
1176
1177
1178 template <int vectorization_width>
1179 void
1180 collect_faces_vectorization(
1181 const std::vector<FaceToCellTopology<1>> &faces_in,
1182 const std::vector<bool> &hard_vectorization_boundary,
1183 std::vector<unsigned int> &face_partition_data,
1184 std::vector<FaceToCellTopology<vectorization_width>> &faces_out,
1185 const std::vector<unsigned int> &active_fe_indices)
1186 {
1187 FaceToCellTopology<vectorization_width> face_batch;
1188 std::vector<std::vector<unsigned int>> faces_type;
1189
1190 unsigned int face_start = face_partition_data[0],
1191 face_end = face_partition_data[0];
1192
1193 face_partition_data[0] = faces_out.size();
1194 for (unsigned int partition = 0;
1195 partition < face_partition_data.size() - 1;
1196 ++partition)
1197 {
1198 std::vector<std::vector<unsigned int>> new_faces_type;
1199
1200 // start with the end point for the last partition
1201 face_start = face_end;
1202 face_end = face_partition_data[partition + 1];
1203
1204 // set the partitioner to the new vectorized lengths
1205 face_partition_data[partition + 1] = face_partition_data[partition];
1206
1207 // loop over the faces in the current partition and reorder according
1208 // to the face type
1209 for (unsigned int face = face_start; face < face_end; ++face)
1210 {
1211 for (auto &face_type : faces_type)
1212 {
1213 // Compare current face with first face of type type
1214 if (compare_faces_for_vectorization(faces_in[face],
1215 faces_in[face_type[0]],
1216 active_fe_indices,
1217 vectorization_width))
1218 {
1219 face_type.push_back(face);
1220 goto face_found;
1221 }
1222 }
1223 faces_type.emplace_back(1, face);
1224 face_found:
1225 {}
1226 }
1227
1228 // insert new faces in sorted list to get good data locality
1229 FaceComparator<vectorization_width> face_comparator(
1230 active_fe_indices);
1231 std::set<FaceToCellTopology<vectorization_width>,
1232 FaceComparator<vectorization_width>>
1233 new_faces(face_comparator);
1234 for (const auto &face_type : faces_type)
1235 {
1236 face_batch.face_type = faces_in[face_type[0]].face_type;
1237 face_batch.interior_face_no =
1238 faces_in[face_type[0]].interior_face_no;
1239 face_batch.exterior_face_no =
1240 faces_in[face_type[0]].exterior_face_no;
1241 face_batch.subface_index = faces_in[face_type[0]].subface_index;
1242 face_batch.face_orientation =
1243 faces_in[face_type[0]].face_orientation;
1244 unsigned int no_faces = face_type.size();
1245 std::vector<unsigned char> touched(no_faces, 0);
1246
1247 // do two passes through the data. The first is to identify
1248 // similar faces within the same index range as the cells which
1249 // will allow for vectorized read operations, the second picks up
1250 // all the rest
1251 unsigned int n_vectorized = 0;
1252 for (unsigned int f = 0; f < no_faces; ++f)
1253 if (faces_in[face_type[f]].cells_interior[0] %
1254 vectorization_width ==
1255 0)
1256 {
1257 bool is_contiguous = true;
1258 if (f + vectorization_width > no_faces)
1259 is_contiguous = false;
1260 else
1261 for (unsigned int v = 1; v < vectorization_width; ++v)
1262 if (faces_in[face_type[f + v]].cells_interior[0] !=
1263 faces_in[face_type[f]].cells_interior[0] + v)
1264 is_contiguous = false;
1265 if (is_contiguous)
1266 {
1267 AssertIndexRange(f,
1268 face_type.size() -
1269 vectorization_width + 1);
1270 for (unsigned int v = 0; v < vectorization_width; ++v)
1271 {
1272 face_batch.cells_interior[v] =
1273 faces_in[face_type[f + v]].cells_interior[0];
1274 face_batch.cells_exterior[v] =
1275 faces_in[face_type[f + v]].cells_exterior[0];
1276 touched[f + v] = 1;
1277 }
1278 new_faces.insert(face_batch);
1279 f += vectorization_width - 1;
1280 n_vectorized += vectorization_width;
1281 }
1282 }
1283
1284 std::vector<unsigned int> untouched;
1285 untouched.reserve(no_faces - n_vectorized);
1286 for (unsigned int f = 0; f < no_faces; ++f)
1287 if (touched[f] == 0)
1288 untouched.push_back(f);
1289 unsigned int v = 0;
1290 for (const auto f : untouched)
1291 {
1292 face_batch.cells_interior[v] =
1293 faces_in[face_type[f]].cells_interior[0];
1294 face_batch.cells_exterior[v] =
1295 faces_in[face_type[f]].cells_exterior[0];
1296 ++v;
1297 if (v == vectorization_width)
1298 {
1299 new_faces.insert(face_batch);
1300 v = 0;
1301 }
1302 }
1303 if (v > 0 && v < vectorization_width)
1304 {
1305 // must add non-filled face
1306 if (hard_vectorization_boundary[partition + 1] ||
1307 partition == face_partition_data.size() - 2)
1308 {
1309 for (; v < vectorization_width; ++v)
1310 {
1311 // Dummy cell, not used
1312 face_batch.cells_interior[v] =
1313 numbers::invalid_unsigned_int;
1314 face_batch.cells_exterior[v] =
1315 numbers::invalid_unsigned_int;
1316 }
1317 new_faces.insert(face_batch);
1318 }
1319 else
1320 {
1321 // postpone to the next partition
1322 std::vector<unsigned int> untreated(v);
1323 for (unsigned int f = 0; f < v; ++f)
1324 untreated[f] = face_type[*(untouched.end() - 1 - f)];
1325 new_faces_type.push_back(untreated);
1326 }
1327 }
1328 }
1329
1330 // insert sorted list to vector of faces
1331 for (auto it = new_faces.begin(); it != new_faces.end(); ++it)
1332 faces_out.push_back(*it);
1333 face_partition_data[partition + 1] += new_faces.size();
1334
1335 // set the faces that were left over to faces_type for the next round
1336 faces_type = std::move(new_faces_type);
1337 }
1338
1339# ifdef DEBUG
1340 // final safety checks
1341 for (const auto &face_type : faces_type)
1342 AssertDimension(face_type.size(), 0U);
1343
1344 AssertDimension(faces_out.size(), face_partition_data.back());
1345 unsigned int nfaces = 0;
1346 for (unsigned int i = face_partition_data[0];
1347 i < face_partition_data.back();
1348 ++i)
1349 for (unsigned int v = 0; v < vectorization_width; ++v)
1350 nfaces +=
1351 (faces_out[i].cells_interior[v] != numbers::invalid_unsigned_int);
1352 AssertDimension(nfaces, faces_in.size());
1353
1354 std::vector<std::pair<unsigned int, unsigned int>> in_faces, out_faces;
1355 for (const auto &face_in : faces_in)
1356 in_faces.emplace_back(face_in.cells_interior[0],
1357 face_in.cells_exterior[0]);
1358 for (unsigned int i = face_partition_data[0];
1359 i < face_partition_data.back();
1360 ++i)
1361 for (unsigned int v = 0;
1362 v < vectorization_width &&
1363 faces_out[i].cells_interior[v] != numbers::invalid_unsigned_int;
1364 ++v)
1365 out_faces.emplace_back(faces_out[i].cells_interior[v],
1366 faces_out[i].cells_exterior[v]);
1367 std::sort(in_faces.begin(), in_faces.end());
1368 std::sort(out_faces.begin(), out_faces.end());
1369 AssertDimension(in_faces.size(), out_faces.size());
1370 for (unsigned int i = 0; i < in_faces.size(); ++i)
1371 {
1372 AssertDimension(in_faces[i].first, out_faces[i].first);
1373 AssertDimension(in_faces[i].second, out_faces[i].second);
1374 }
1375# endif
1376 }
1377
1378#endif // ifndef DOXYGEN
1379
1380 } // namespace MatrixFreeFunctions
1381} // namespace internal
1382
1383
1384DEAL_II_NAMESPACE_CLOSE
1385
1386#endif
MPI_Comm
Triangulation::n_raw_faces
unsigned int n_raw_faces() const
Triangulation::is_mixed_mesh
bool is_mixed_mesh() const
parallel::TriangulationBase::locally_owned_subdomain
types::subdomain_id locally_owned_subdomain() const override
Definition tria_base.cc:345
DEAL_II_NAMESPACE_OPEN
#define DEAL_II_NAMESPACE_OPEN
Definition config.h:503
DEAL_II_NAMESPACE_CLOSE
#define DEAL_II_NAMESPACE_CLOSE
Definition config.h:504
face_info.h
second
Point< 2 > second
Definition grid_out.cc:4624
first
Point< 2 > first
Definition grid_out.cc:4623
StandardExceptions::ExcNotImplemented
static ::ExceptionBase & ExcNotImplemented()
Assert
#define Assert(cond, exc)
Definition exceptions.h:1638
AssertDimension
#define AssertDimension(dim1, dim2)
Definition exceptions.h:1985
AssertThrowMPI
#define AssertThrowMPI(error_code)
Definition exceptions.h:2112
AssertIndexRange
#define AssertIndexRange(index, range)
Definition exceptions.h:2053
StandardExceptions::ExcInternalError
static ::ExceptionBase & ExcInternalError()
StandardExceptions::ExcMessage
static ::ExceptionBase & ExcMessage(std::string arg1)
AssertThrow
#define AssertThrow(cond, exc)
Definition exceptions.h:1739
memory_consumption.h
ReferenceCells::get_hypercube
constexpr const ReferenceCell & get_hypercube()
Definition reference_cell.h:2557
SparsityTools::partition
void partition(const SparsityPattern &sparsity_pattern, const unsigned int n_partitions, std::vector< unsigned int > &partition_indices, const Partitioner partitioner=Partitioner::metis)
Definition sparsity_tools.cc:398
internal::MatrixFreeFunctions::collect_faces_vectorization
void collect_faces_vectorization(const std::vector< FaceToCellTopology< 1 > > &faces_in, const std::vector< bool > &hard_vectorization_boundary, std::vector< unsigned int > &face_partition_data, std::vector< FaceToCellTopology< vectorization_width > > &faces_out)
internal::split_face_orientation
std::tuple< bool, bool, bool > split_face_orientation(const unsigned char combined_face_orientation)
Definition tria_orientation.h:45
numbers::invalid_subdomain_id
const types::subdomain_id invalid_subdomain_id
Definition types.h:341
numbers::invalid_unsigned_int
static const unsigned int invalid_unsigned_int
Definition types.h:220
triangulation
const ::parallel::distributed::Triangulation< dim, spacedim > * triangulation
Definition p4est_wrappers.cc:68
comm
*braid_SplitCommworld & comm
Definition parallel_in_time.h:1981
shape_info.h
internal::MatrixFreeFunctions::FaceIdentifier::shared_faces
std::vector< std::pair< CellId, CellId > > shared_faces
Definition face_setup_internal.h:53
internal::MatrixFreeFunctions::FaceSetup::inner_faces
std::vector< FaceToCellTopology< 1 > > inner_faces
Definition face_setup_internal.h:131
internal::MatrixFreeFunctions::FaceSetup::boundary_faces
std::vector< FaceToCellTopology< 1 > > boundary_faces
Definition face_setup_internal.h:132
internal::MatrixFreeFunctions::FaceSetup::refinement_edge_faces
std::vector< FaceToCellTopology< 1 > > refinement_edge_faces
Definition face_setup_internal.h:134
internal::MatrixFreeFunctions::FaceSetup::create_face
FaceToCellTopology< 1 > create_face(const unsigned int face_no, const typename ::Triangulation< dim >::cell_iterator &cell, const unsigned int number_cell_interior, const typename ::Triangulation< dim >::cell_iterator &neighbor, const unsigned int number_cell_exterior, const bool is_mixed_mesh)
internal::MatrixFreeFunctions::FaceSetup::initialize
void initialize(const ::Triangulation< dim > &triangulation, const unsigned int mg_level, const bool hold_all_faces_to_owned_cells, const bool build_inner_faces, std::vector< std::pair< unsigned int, unsigned int > > &cell_levels)
internal::MatrixFreeFunctions::FaceSetup::inner_ghost_faces
std::vector< FaceToCellTopology< 1 > > inner_ghost_faces
Definition face_setup_internal.h:133
internal::MatrixFreeFunctions::FaceSetup::generate_faces
void generate_faces(const ::Triangulation< dim > &triangulation, const std::vector< std::pair< unsigned int, unsigned int > > &cell_levels, TaskInfo &task_info)
task_info.h
tria_accessor.h
tria_base.h
Generated by doxygen 1.11.0