/[escript]/branches/ripleygmg_from_3668/ripley/src/Brick.cpp
ViewVC logotype

Diff of /branches/ripleygmg_from_3668/ripley/src/Brick.cpp

Parent Directory Parent Directory | Revision Log Revision Log | View Patch Patch

revision 3703 by caltinay, Sun Dec 4 23:42:52 2011 UTC revision 3760 by caltinay, Mon Jan 9 05:21:18 2012 UTC
# Line 13  Line 13 
13    
14  #include <ripley/Brick.h>  #include <ripley/Brick.h>
15  extern "C" {  extern "C" {
16  #include "paso/SystemMatrixPattern.h"  #include "paso/SystemMatrix.h"
17  }  }
18    
19  #if USE_SILO  #if USE_SILO
# Line 47  Brick::Brick(int n0, int n1, int n2, dou Line 47  Brick::Brick(int n0, int n1, int n2, dou
47      if (m_NX*m_NY*m_NZ != m_mpiInfo->size)      if (m_NX*m_NY*m_NZ != m_mpiInfo->size)
48          throw RipleyException("Invalid number of spatial subdivisions");          throw RipleyException("Invalid number of spatial subdivisions");
49    
50      if (n0%m_NX > 0 || n1%m_NY > 0 || n2%m_NZ > 0)      if ((n0+1)%m_NX > 0 || (n1+1)%m_NY > 0 || (n2+1)%m_NZ > 0)
51          throw RipleyException("Number of elements must be separable into number of ranks in each dimension");          throw RipleyException("Number of elements+1 must be separable into number of ranks in each dimension");
52    
53      // local number of elements      if ((m_NX > 1 && (n0+1)/m_NX<2) || (m_NY > 1 && (n1+1)/m_NY<2) || (m_NZ > 1 && (n2+1)/m_NZ<2))
54      m_NE0 = n0/m_NX;          throw RipleyException("Too few elements for the number of ranks");
55      m_NE1 = n1/m_NY;  
56      m_NE2 = n2/m_NZ;      // local number of elements (including overlap)
57      // local number of nodes (not necessarily owned)      m_NE0 = (m_NX>1 ? (n0+1)/m_NX : n0);
58        if (m_mpiInfo->rank%m_NX>0 && m_mpiInfo->rank%m_NX<m_NX-1)
59            m_NE0++;
60        m_NE1 = (m_NY>1 ? (n1+1)/m_NY : n1);
61        if (m_mpiInfo->rank%(m_NX*m_NY)/m_NX>0 && m_mpiInfo->rank%(m_NX*m_NY)/m_NX<m_NY-1)
62            m_NE1++;
63        m_NE2 = (m_NZ>1 ? (n2+1)/m_NZ : n2);
64        if (m_mpiInfo->rank/(m_NX*m_NY)>0 && m_mpiInfo->rank/(m_NX*m_NY)<m_NZ-1)
65            m_NE2++;
66    
67        // local number of nodes
68      m_N0 = m_NE0+1;      m_N0 = m_NE0+1;
69      m_N1 = m_NE1+1;      m_N1 = m_NE1+1;
70      m_N2 = m_NE2+1;      m_N2 = m_NE2+1;
71    
72      // bottom-left-front node is at (offset0,offset1,offset2) in global mesh      // bottom-left-front node is at (offset0,offset1,offset2) in global mesh
73      m_offset0 = m_NE0*(m_mpiInfo->rank%m_NX);      m_offset0 = (n0+1)/m_NX*(m_mpiInfo->rank%m_NX);
74      m_offset1 = m_NE1*(m_mpiInfo->rank%(m_NX*m_NY)/m_NX);      if (m_offset0 > 0)
75      m_offset2 = m_NE2*(m_mpiInfo->rank/(m_NX*m_NY));          m_offset0--;
76        m_offset1 = (n1+1)/m_NY*(m_mpiInfo->rank%(m_NX*m_NY)/m_NX);
77        if (m_offset1 > 0)
78            m_offset1--;
79        m_offset2 = (n2+1)/m_NZ*(m_mpiInfo->rank/(m_NX*m_NY));
80        if (m_offset2 > 0)
81            m_offset2--;
82    
83      populateSampleIds();      populateSampleIds();
84        createPattern();
85  }  }
86    
87    
# Line 77  string Brick::getDescription() const Line 96  string Brick::getDescription() const
96    
97  bool Brick::operator==(const AbstractDomain& other) const  bool Brick::operator==(const AbstractDomain& other) const
98  {  {
99      if (dynamic_cast<const Brick*>(&other))      const Brick* o=dynamic_cast<const Brick*>(&other);
100          return this==&other;      if (o) {
101            return (RipleyDomain::operator==(other) &&
102                    m_gNE0==o->m_gNE0 && m_gNE1==o->m_gNE1 && m_gNE2==o->m_gNE2
103                    && m_l0==o->m_l0 && m_l1==o->m_l1 && m_l2==o->m_l2
104                    && m_NX==o->m_NX && m_NY==o->m_NY && m_NZ==o->m_NZ);
105        }
106    
107      return false;      return false;
108  }  }
# Line 232  const int* Brick::borrowSampleReferenceI Line 256  const int* Brick::borrowSampleReferenceI
256  {  {
257      switch (fsType) {      switch (fsType) {
258          case Nodes:          case Nodes:
259            case ReducedNodes: //FIXME: reduced
260              return &m_nodeId[0];              return &m_nodeId[0];
261            case DegreesOfFreedom:
262            case ReducedDegreesOfFreedom: //FIXME: reduced
263                return &m_dofId[0];
264          case Elements:          case Elements:
265            case ReducedElements:
266              return &m_elementId[0];              return &m_elementId[0];
267          case FaceElements:          case FaceElements:
268            case ReducedFaceElements:
269              return &m_faceId[0];              return &m_faceId[0];
270          default:          default:
271              break;              break;
# Line 247  const int* Brick::borrowSampleReferenceI Line 277  const int* Brick::borrowSampleReferenceI
277      throw RipleyException(msg.str());      throw RipleyException(msg.str());
278  }  }
279    
280  bool Brick::ownSample(int fsCode, index_t id) const  bool Brick::ownSample(int fsType, index_t id) const
281  {  {
282  #ifdef ESYS_MPI      if (getMPISize()==1)
283      if (fsCode == Nodes) {          return true;
284          const index_t myFirst=m_nodeDistribution[m_mpiInfo->rank];  
285          const index_t myLast=m_nodeDistribution[m_mpiInfo->rank+1]-1;      switch (fsType) {
286          return (m_nodeId[id]>=myFirst && m_nodeId[id]<=myLast);          case Nodes:
287      } else          case ReducedNodes: //FIXME: reduced
288          throw RipleyException("ownSample() only implemented for Nodes");              return (m_dofMap[id] < getNumDOF());
289  #else          case DegreesOfFreedom:
290      return true;          case ReducedDegreesOfFreedom:
291  #endif              return true;
292            case Elements:
293            case ReducedElements:
294                {
295                    // check ownership of element's _last_ node
296                    const index_t x=id%m_NE0 + 1;
297                    const index_t y=id%(m_NE0*m_NE1)/m_NE0 + 1;
298                    const index_t z=id/(m_NE0*m_NE1) + 1;
299                    return (m_dofMap[x + m_N0*y +m_N0*m_N1*z] < getNumDOF());
300                }
301            case FaceElements:
302            case ReducedFaceElements:
303                {
304                    // check ownership of face element's last node
305                    const IndexVector faces = getNumFacesPerBoundary();
306                    dim_t n=0;
307                    for (size_t i=0; i<faces.size(); i++) {
308                        n+=faces[i];
309                        if (id<n) {
310                            const index_t j=id-n+faces[i];
311                            if (i>=4) { // front or back
312                                const index_t first=(i==4 ? 0 : m_N0*m_N1*(m_N2-1));
313                                return (m_dofMap[first+j%m_NE0+1+(j/m_NE0+1)*m_N0] < getNumDOF());
314                            } else if (i>=2) { // bottom or top
315                                const index_t first=(i==2 ? 0 : m_N0*(m_N1-1));
316                                return (m_dofMap[first+j%m_NE0+1+(j/m_NE0+1)*m_N0*m_N1] < getNumDOF());
317                            } else { // left or right
318                                const index_t first=(i==0 ? 0 : m_N0-1);
319                                return (m_dofMap[first+(j%m_NE1+1)*m_N0+(j/m_NE1+1)*m_N0*m_N1] < getNumDOF());
320                            }
321                        }
322                    }
323                    return false;
324                }
325            default:
326                break;
327        }
328    
329        stringstream msg;
330        msg << "ownSample() not implemented for "
331            << functionSpaceTypeAsString(fsType);
332        throw RipleyException(msg.str());
333  }  }
334    
335  void Brick::setToGradient(escript::Data& out, const escript::Data& cIn) const  void Brick::setToGradient(escript::Data& out, const escript::Data& cIn) const
# Line 268  void Brick::setToGradient(escript::Data& Line 339  void Brick::setToGradient(escript::Data&
339      const double h0 = m_l0/m_gNE0;      const double h0 = m_l0/m_gNE0;
340      const double h1 = m_l1/m_gNE1;      const double h1 = m_l1/m_gNE1;
341      const double h2 = m_l1/m_gNE2;      const double h2 = m_l1/m_gNE2;
342        const double C0 = .044658198738520451079;
343        const double C1 = .16666666666666666667;
344        const double C2 = .21132486540518711775;
345        const double C3 = .25;
346        const double C4 = .5;
347        const double C5 = .62200846792814621559;
348        const double C6 = .78867513459481288225;
349    
350      if (out.getFunctionSpace().getTypeCode() == Elements) {      if (out.getFunctionSpace().getTypeCode() == Elements) {
351          /* GENERATOR SNIP_GRAD_ELEMENTS TOP */          out.requireWrite();
352          const double tmp0_22 = -0.044658198738520451079/h1;          /*** GENERATOR SNIP_GRAD_ELEMENTS TOP */
         const double tmp0_16 = 0.16666666666666666667/h0;  
         const double tmp0_33 = -0.62200846792814621559/h1;  
         const double tmp0_0 = -0.62200846792814621559/h0;  
         const double tmp0_21 = -0.16666666666666666667/h1;  
         const double tmp0_17 = 0.62200846792814621559/h0;  
         const double tmp0_52 = -0.044658198738520451079/h2;  
         const double tmp0_1 = -0.16666666666666666667/h0;  
         const double tmp0_20 = -0.62200846792814621559/h1;  
         const double tmp0_14 = -0.044658198738520451079/h0;  
         const double tmp0_53 = -0.62200846792814621559/h2;  
         const double tmp0_49 = 0.16666666666666666667/h2;  
         const double tmp0_2 = 0.16666666666666666667/h0;  
         const double tmp0_27 = -0.044658198738520451079/h1;  
         const double tmp0_15 = -0.16666666666666666667/h0;  
         const double tmp0_50 = -0.16666666666666666667/h2;  
         const double tmp0_48 = 0.62200846792814621559/h2;  
         const double tmp0_3 = 0.044658198738520451079/h0;  
         const double tmp0_26 = -0.16666666666666666667/h1;  
         const double tmp0_12 = -0.62200846792814621559/h0;  
         const double tmp0_51 = 0.044658198738520451079/h2;  
         const double tmp0_25 = 0.62200846792814621559/h1;  
         const double tmp0_13 = 0.16666666666666666667/h0;  
         const double tmp0_56 = 0.16666666666666666667/h2;  
         const double tmp0_24 = 0.16666666666666666667/h1;  
         const double tmp0_10 = 0.62200846792814621559/h0;  
         const double tmp0_57 = 0.62200846792814621559/h2;  
         const double tmp0_11 = -0.16666666666666666667/h0;  
         const double tmp0_54 = -0.044658198738520451079/h2;  
         const double tmp0_38 = 0.16666666666666666667/h1;  
         const double tmp0_34 = -0.044658198738520451079/h1;  
         const double tmp0_42 = 0.16666666666666666667/h2;  
         const double tmp0_35 = -0.16666666666666666667/h1;  
         const double tmp0_36 = -0.62200846792814621559/h1;  
         const double tmp0_41 = 0.62200846792814621559/h2;  
         const double tmp0_8 = 0.044658198738520451079/h0;  
         const double tmp0_37 = 0.62200846792814621559/h1;  
         const double tmp0_29 = 0.16666666666666666667/h1;  
         const double tmp0_40 = -0.62200846792814621559/h2;  
         const double tmp0_9 = 0.16666666666666666667/h0;  
         const double tmp0_30 = 0.62200846792814621559/h1;  
         const double tmp0_28 = -0.16666666666666666667/h1;  
         const double tmp0_43 = 0.044658198738520451079/h2;  
         const double tmp0_32 = 0.16666666666666666667/h1;  
         const double tmp0_31 = 0.044658198738520451079/h1;  
         const double tmp0_39 = 0.044658198738520451079/h1;  
         const double tmp0_58 = -0.62200846792814621559/h2;  
         const double tmp0_55 = 0.044658198738520451079/h2;  
         const double tmp0_18 = -0.62200846792814621559/h0;  
         const double tmp0_45 = -0.16666666666666666667/h2;  
         const double tmp0_59 = -0.16666666666666666667/h2;  
         const double tmp0_4 = -0.044658198738520451079/h0;  
         const double tmp0_19 = 0.044658198738520451079/h0;  
         const double tmp0_44 = -0.044658198738520451079/h2;  
         const double tmp0_5 = 0.62200846792814621559/h0;  
         const double tmp0_47 = 0.16666666666666666667/h2;  
         const double tmp0_6 = -0.16666666666666666667/h0;  
         const double tmp0_23 = 0.044658198738520451079/h1;  
         const double tmp0_46 = -0.16666666666666666667/h2;  
         const double tmp0_7 = -0.044658198738520451079/h0;  
353  #pragma omp parallel for  #pragma omp parallel for
354          for (index_t k2 =0; k2 < m_NE2; ++k2) {          for (index_t k2=0; k2 < m_NE2; ++k2) {
355              for (index_t k1 =0; k1 < m_NE1; ++k1) {              for (index_t k1=0; k1 < m_NE1; ++k1) {
356                  for (index_t k0 =0; k0 < m_NE0; ++k0) {                  for (index_t k0=0; k0 < m_NE0; ++k0) {
357                      const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,k2, m_N0,m_N1));                      const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,k2, m_N0,m_N1));
358                      const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,k2+1, m_N0,m_N1));                      const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,k2+1, m_N0,m_N1));
359                      const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,k2+1, m_N0,m_N1));                      const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,k2+1, m_N0,m_N1));
# Line 344  void Brick::setToGradient(escript::Data& Line 364  void Brick::setToGradient(escript::Data&
364                      const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,k2, m_N0,m_N1));                      const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,k2, m_N0,m_N1));
365                      double* o = out.getSampleDataRW(INDEX3(k0,k1,k2,m_NE0,m_NE1));                      double* o = out.getSampleDataRW(INDEX3(k0,k1,k2,m_NE0,m_NE1));
366                      for (index_t i=0; i < numComp; ++i) {                      for (index_t i=0; i < numComp; ++i) {
367                          o[INDEX3(i,0,0,numComp,3)] = f_000[i]*tmp0_0 + f_011[i]*tmp0_4 + f_100[i]*tmp0_5 + f_111[i]*tmp0_3 + tmp0_1*(f_001[i] + f_010[i]) + tmp0_2*(f_101[i] + f_110[i]);                          const double V0=((f_100[i]-f_000[i])*C5 + (f_111[i]-f_011[i])*C0 + (f_101[i]+f_110[i]-f_001[i]-f_010[i])*C1) / h0;
368                          o[INDEX3(i,1,0,numComp,3)] = f_000[i]*tmp0_20 + f_010[i]*tmp0_25 + f_101[i]*tmp0_22 + f_111[i]*tmp0_23 + tmp0_21*(f_001[i] + f_100[i]) + tmp0_24*(f_011[i] + f_110[i]);                          const double V1=((f_110[i]-f_010[i])*C5 + (f_101[i]-f_001[i])*C0 + (f_100[i]+f_111[i]-f_000[i]-f_011[i])*C1) / h0;
369                          o[INDEX3(i,2,0,numComp,3)] = f_000[i]*tmp0_40 + f_001[i]*tmp0_41 + f_110[i]*tmp0_44 + f_111[i]*tmp0_43 + tmp0_42*(f_011[i] + f_101[i]) + tmp0_45*(f_010[i] + f_100[i]);                          const double V2=((f_101[i]-f_001[i])*C5 + (f_110[i]-f_010[i])*C0 + (f_100[i]+f_111[i]-f_000[i]-f_011[i])*C1) / h0;
370                          o[INDEX3(i,0,1,numComp,3)] = f_000[i]*tmp0_0 + f_011[i]*tmp0_4 + f_100[i]*tmp0_5 + f_111[i]*tmp0_3 + tmp0_1*(f_001[i] + f_010[i]) + tmp0_2*(f_101[i] + f_110[i]);                          const double V3=((f_111[i]-f_011[i])*C5 + (f_100[i]-f_000[i])*C0 + (f_101[i]+f_110[i]-f_001[i]-f_010[i])*C1) / h0;
371                          o[INDEX3(i,1,1,numComp,3)] = f_000[i]*tmp0_26 + f_001[i]*tmp0_27 + f_010[i]*tmp0_32 + f_011[i]*tmp0_31 + f_100[i]*tmp0_33 + f_101[i]*tmp0_28 + f_110[i]*tmp0_30 + f_111[i]*tmp0_29;                          const double V4=((f_010[i]-f_000[i])*C5 + (f_111[i]-f_101[i])*C0 + (f_011[i]+f_110[i]-f_001[i]-f_100[i])*C1) / h1;
372                          o[INDEX3(i,2,1,numComp,3)] = f_000[i]*tmp0_46 + f_001[i]*tmp0_47 + f_010[i]*tmp0_52 + f_011[i]*tmp0_51 + f_100[i]*tmp0_53 + f_101[i]*tmp0_48 + f_110[i]*tmp0_50 + f_111[i]*tmp0_49;                          const double V5=((f_110[i]-f_100[i])*C5 + (f_011[i]-f_001[i])*C0 + (f_010[i]+f_111[i]-f_000[i]-f_101[i])*C1) / h1;
373                          o[INDEX3(i,0,2,numComp,3)] = f_000[i]*tmp0_6 + f_001[i]*tmp0_7 + f_010[i]*tmp0_12 + f_011[i]*tmp0_11 + f_100[i]*tmp0_13 + f_101[i]*tmp0_8 + f_110[i]*tmp0_10 + f_111[i]*tmp0_9;                          const double V6=((f_011[i]-f_001[i])*C5 + (f_110[i]-f_100[i])*C0 + (f_010[i]+f_111[i]-f_000[i]-f_101[i])*C1) / h1;
374                          o[INDEX3(i,1,2,numComp,3)] = f_000[i]*tmp0_20 + f_010[i]*tmp0_25 + f_101[i]*tmp0_22 + f_111[i]*tmp0_23 + tmp0_21*(f_001[i] + f_100[i]) + tmp0_24*(f_011[i] + f_110[i]);                          const double V7=((f_111[i]-f_101[i])*C5 + (f_010[i]-f_000[i])*C0 + (f_011[i]+f_110[i]-f_001[i]-f_100[i])*C1) / h1;
375                          o[INDEX3(i,2,2,numComp,3)] = f_000[i]*tmp0_46 + f_001[i]*tmp0_47 + f_010[i]*tmp0_53 + f_011[i]*tmp0_48 + f_100[i]*tmp0_52 + f_101[i]*tmp0_51 + f_110[i]*tmp0_50 + f_111[i]*tmp0_49;                          const double V8=((f_001[i]-f_000[i])*C5 + (f_111[i]-f_110[i])*C0 + (f_011[i]+f_101[i]-f_010[i]-f_100[i])*C1) / h2;
376                          o[INDEX3(i,0,3,numComp,3)] = f_000[i]*tmp0_6 + f_001[i]*tmp0_7 + f_010[i]*tmp0_12 + f_011[i]*tmp0_11 + f_100[i]*tmp0_13 + f_101[i]*tmp0_8 + f_110[i]*tmp0_10 + f_111[i]*tmp0_9;                          const double V9=((f_101[i]-f_100[i])*C5 + (f_011[i]-f_010[i])*C0 + (f_001[i]+f_111[i]-f_000[i]-f_110[i])*C1) / h2;
377                          o[INDEX3(i,1,3,numComp,3)] = f_000[i]*tmp0_26 + f_001[i]*tmp0_27 + f_010[i]*tmp0_32 + f_011[i]*tmp0_31 + f_100[i]*tmp0_33 + f_101[i]*tmp0_28 + f_110[i]*tmp0_30 + f_111[i]*tmp0_29;                          const double V10=((f_011[i]-f_010[i])*C5 + (f_101[i]-f_100[i])*C0 + (f_001[i]+f_111[i]-f_000[i]-f_110[i])*C1) / h2;
378                          o[INDEX3(i,2,3,numComp,3)] = f_000[i]*tmp0_54 + f_001[i]*tmp0_55 + f_110[i]*tmp0_58 + f_111[i]*tmp0_57 + tmp0_56*(f_011[i] + f_101[i]) + tmp0_59*(f_010[i] + f_100[i]);                          const double V11=((f_111[i]-f_110[i])*C5 + (f_001[i]-f_000[i])*C0 + (f_011[i]+f_101[i]-f_010[i]-f_100[i])*C1) / h2;
379                          o[INDEX3(i,0,4,numComp,3)] = f_000[i]*tmp0_6 + f_001[i]*tmp0_12 + f_010[i]*tmp0_7 + f_011[i]*tmp0_11 + f_100[i]*tmp0_13 + f_101[i]*tmp0_10 + f_110[i]*tmp0_8 + f_111[i]*tmp0_9;                          o[INDEX3(i,0,0,numComp,3)] = V0;
380                          o[INDEX3(i,1,4,numComp,3)] = f_000[i]*tmp0_26 + f_001[i]*tmp0_33 + f_010[i]*tmp0_32 + f_011[i]*tmp0_30 + f_100[i]*tmp0_27 + f_101[i]*tmp0_28 + f_110[i]*tmp0_31 + f_111[i]*tmp0_29;                          o[INDEX3(i,1,0,numComp,3)] = V4;
381                          o[INDEX3(i,2,4,numComp,3)] = f_000[i]*tmp0_40 + f_001[i]*tmp0_41 + f_110[i]*tmp0_44 + f_111[i]*tmp0_43 + tmp0_42*(f_011[i] + f_101[i]) + tmp0_45*(f_010[i] + f_100[i]);                          o[INDEX3(i,2,0,numComp,3)] = V8;
382                          o[INDEX3(i,0,5,numComp,3)] = f_000[i]*tmp0_6 + f_001[i]*tmp0_12 + f_010[i]*tmp0_7 + f_011[i]*tmp0_11 + f_100[i]*tmp0_13 + f_101[i]*tmp0_10 + f_110[i]*tmp0_8 + f_111[i]*tmp0_9;                          o[INDEX3(i,0,1,numComp,3)] = V0;
383                          o[INDEX3(i,1,5,numComp,3)] = f_000[i]*tmp0_34 + f_010[i]*tmp0_39 + f_101[i]*tmp0_36 + f_111[i]*tmp0_37 + tmp0_35*(f_001[i] + f_100[i]) + tmp0_38*(f_011[i] + f_110[i]);                          o[INDEX3(i,1,1,numComp,3)] = V5;
384                          o[INDEX3(i,2,5,numComp,3)] = f_000[i]*tmp0_46 + f_001[i]*tmp0_47 + f_010[i]*tmp0_52 + f_011[i]*tmp0_51 + f_100[i]*tmp0_53 + f_101[i]*tmp0_48 + f_110[i]*tmp0_50 + f_111[i]*tmp0_49;                          o[INDEX3(i,2,1,numComp,3)] = V9;
385                          o[INDEX3(i,0,6,numComp,3)] = f_000[i]*tmp0_14 + f_011[i]*tmp0_18 + f_100[i]*tmp0_19 + f_111[i]*tmp0_17 + tmp0_15*(f_001[i] + f_010[i]) + tmp0_16*(f_101[i] + f_110[i]);                          o[INDEX3(i,0,2,numComp,3)] = V1;
386                          o[INDEX3(i,1,6,numComp,3)] = f_000[i]*tmp0_26 + f_001[i]*tmp0_33 + f_010[i]*tmp0_32 + f_011[i]*tmp0_30 + f_100[i]*tmp0_27 + f_101[i]*tmp0_28 + f_110[i]*tmp0_31 + f_111[i]*tmp0_29;                          o[INDEX3(i,1,2,numComp,3)] = V4;
387                          o[INDEX3(i,2,6,numComp,3)] = f_000[i]*tmp0_46 + f_001[i]*tmp0_47 + f_010[i]*tmp0_53 + f_011[i]*tmp0_48 + f_100[i]*tmp0_52 + f_101[i]*tmp0_51 + f_110[i]*tmp0_50 + f_111[i]*tmp0_49;                          o[INDEX3(i,2,2,numComp,3)] = V10;
388                          o[INDEX3(i,0,7,numComp,3)] = f_000[i]*tmp0_14 + f_011[i]*tmp0_18 + f_100[i]*tmp0_19 + f_111[i]*tmp0_17 + tmp0_15*(f_001[i] + f_010[i]) + tmp0_16*(f_101[i] + f_110[i]);                          o[INDEX3(i,0,3,numComp,3)] = V1;
389                          o[INDEX3(i,1,7,numComp,3)] = f_000[i]*tmp0_34 + f_010[i]*tmp0_39 + f_101[i]*tmp0_36 + f_111[i]*tmp0_37 + tmp0_35*(f_001[i] + f_100[i]) + tmp0_38*(f_011[i] + f_110[i]);                          o[INDEX3(i,1,3,numComp,3)] = V5;
390                          o[INDEX3(i,2,7,numComp,3)] = f_000[i]*tmp0_54 + f_001[i]*tmp0_55 + f_110[i]*tmp0_58 + f_111[i]*tmp0_57 + tmp0_56*(f_011[i] + f_101[i]) + tmp0_59*(f_010[i] + f_100[i]);                          o[INDEX3(i,2,3,numComp,3)] = V11;
391                            o[INDEX3(i,0,4,numComp,3)] = V2;
392                            o[INDEX3(i,1,4,numComp,3)] = V6;
393                            o[INDEX3(i,2,4,numComp,3)] = V8;
394                            o[INDEX3(i,0,5,numComp,3)] = V2;
395                            o[INDEX3(i,1,5,numComp,3)] = V7;
396                            o[INDEX3(i,2,5,numComp,3)] = V9;
397                            o[INDEX3(i,0,6,numComp,3)] = V3;
398                            o[INDEX3(i,1,6,numComp,3)] = V6;
399                            o[INDEX3(i,2,6,numComp,3)] = V10;
400                            o[INDEX3(i,0,7,numComp,3)] = V3;
401                            o[INDEX3(i,1,7,numComp,3)] = V7;
402                            o[INDEX3(i,2,7,numComp,3)] = V11;
403                      } /* end of component loop i */                      } /* end of component loop i */
404                  } /* end of k0 loop */                  } /* end of k0 loop */
405              } /* end of k1 loop */              } /* end of k1 loop */
406          } /* end of k2 loop */          } /* end of k2 loop */
407          /* GENERATOR SNIP_GRAD_ELEMENTS BOTTOM */          /* GENERATOR SNIP_GRAD_ELEMENTS BOTTOM */
408        } else if (out.getFunctionSpace().getTypeCode() == ReducedElements) {
409            out.requireWrite();
410            /*** GENERATOR SNIP_GRAD_REDUCED_ELEMENTS TOP */
411    #pragma omp parallel for
412            for (index_t k2=0; k2 < m_NE2; ++k2) {
413                for (index_t k1=0; k1 < m_NE1; ++k1) {
414                    for (index_t k0=0; k0 < m_NE0; ++k0) {
415                        const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,k2, m_N0,m_N1));
416                        const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,k2+1, m_N0,m_N1));
417                        const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,k2+1, m_N0,m_N1));
418                        const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,k2+1, m_N0,m_N1));
419                        const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,k2, m_N0,m_N1));
420                        const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,k2, m_N0,m_N1));
421                        const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,k2, m_N0,m_N1));
422                        const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,k2+1, m_N0,m_N1));
423                        double* o = out.getSampleDataRW(INDEX3(k0,k1,k2,m_NE0,m_NE1));
424                        for (index_t i=0; i < numComp; ++i) {
425                            o[INDEX3(i,0,0,numComp,3)] = (f_100[i]+f_101[i]+f_110[i]+f_111[i]-f_000[i]-f_001[i]-f_010[i]-f_011[i])*C3 / h0;
426                            o[INDEX3(i,1,0,numComp,3)] = (f_010[i]+f_011[i]+f_110[i]+f_111[i]-f_000[i]-f_001[i]-f_100[i]-f_101[i])*C3 / h1;
427                            o[INDEX3(i,2,0,numComp,3)] = (f_001[i]+f_011[i]+f_101[i]+f_111[i]-f_000[i]-f_010[i]-f_100[i]-f_110[i])*C3 / h2;
428                        } /* end of component loop i */
429                    } /* end of k0 loop */
430                } /* end of k1 loop */
431            } /* end of k2 loop */
432            /* GENERATOR SNIP_GRAD_REDUCED_ELEMENTS BOTTOM */
433        } else if (out.getFunctionSpace().getTypeCode() == FaceElements) {
434            out.requireWrite();
435            /*** GENERATOR SNIP_GRAD_FACES TOP */
436    #pragma omp parallel
437            {
438                if (m_faceOffset[0] > -1) {
439    #pragma omp for nowait
440                    for (index_t k2=0; k2 < m_NE2; ++k2) {
441                        for (index_t k1=0; k1 < m_NE1; ++k1) {
442                            const register double* f_000 = in.getSampleDataRO(INDEX3(0,k1,k2, m_N0,m_N1));
443                            const register double* f_001 = in.getSampleDataRO(INDEX3(0,k1,k2+1, m_N0,m_N1));
444                            const register double* f_101 = in.getSampleDataRO(INDEX3(1,k1,k2+1, m_N0,m_N1));
445                            const register double* f_111 = in.getSampleDataRO(INDEX3(1,k1+1,k2+1, m_N0,m_N1));
446                            const register double* f_110 = in.getSampleDataRO(INDEX3(1,k1+1,k2, m_N0,m_N1));
447                            const register double* f_011 = in.getSampleDataRO(INDEX3(0,k1+1,k2+1, m_N0,m_N1));
448                            const register double* f_010 = in.getSampleDataRO(INDEX3(0,k1+1,k2, m_N0,m_N1));
449                            const register double* f_100 = in.getSampleDataRO(INDEX3(1,k1,k2, m_N0,m_N1));
450                            double* o = out.getSampleDataRW(m_faceOffset[0]+INDEX2(k1,k2,m_NE1));
451                            for (index_t i=0; i < numComp; ++i) {
452                                const double V0=((f_010[i]-f_000[i])*C6 + (f_011[i]-f_001[i])*C2) / h1;
453                                const double V1=((f_010[i]-f_000[i])*C2 + (f_011[i]-f_001[i])*C6) / h1;
454                                const double V2=((f_001[i]-f_000[i])*C6 + (f_010[i]-f_011[i])*C2) / h2;
455                                const double V3=((f_001[i]-f_000[i])*C2 + (f_011[i]-f_010[i])*C6) / h2;
456                                o[INDEX3(i,0,0,numComp,3)] = ((f_100[i]-f_000[i])*C5 + (f_111[i]-f_011[i])*C0 + (f_101[i]+f_110[i]-f_001[i]-f_010[i])*C1) / h0;
457                                o[INDEX3(i,1,0,numComp,3)] = V0;
458                                o[INDEX3(i,2,0,numComp,3)] = V2;
459                                o[INDEX3(i,0,1,numComp,3)] = ((f_110[i]-f_010[i])*C5 + (f_101[i]-f_001[i])*C0 + (f_100[i]+f_111[i]-f_000[i]-f_011[i])*C1) / h0;
460                                o[INDEX3(i,1,1,numComp,3)] = V0;
461                                o[INDEX3(i,2,1,numComp,3)] = V3;
462                                o[INDEX3(i,0,2,numComp,3)] = ((f_101[i]-f_001[i])*C5 + (f_110[i]-f_010[i])*C0 + (f_100[i]+f_111[i]-f_000[i]-f_011[i])*C1) / h0;
463                                o[INDEX3(i,1,2,numComp,3)] = V1;
464                                o[INDEX3(i,2,2,numComp,3)] = V2;
465                                o[INDEX3(i,0,3,numComp,3)] = ((f_111[i]-f_011[i])*C5 + (f_100[i]-f_000[i])*C0 + (f_101[i]+f_110[i]-f_001[i]-f_010[i])*C1) / h0;
466                                o[INDEX3(i,1,3,numComp,3)] = V1;
467                                o[INDEX3(i,2,3,numComp,3)] = V3;
468                            } /* end of component loop i */
469                        } /* end of k1 loop */
470                    } /* end of k2 loop */
471                } /* end of face 0 */
472                if (m_faceOffset[1] > -1) {
473    #pragma omp for nowait
474                    for (index_t k2=0; k2 < m_NE2; ++k2) {
475                        for (index_t k1=0; k1 < m_NE1; ++k1) {
476                            const register double* f_000 = in.getSampleDataRO(INDEX3(m_N0-2,k1,k2, m_N0,m_N1));
477                            const register double* f_001 = in.getSampleDataRO(INDEX3(m_N0-2,k1,k2+1, m_N0,m_N1));
478                            const register double* f_101 = in.getSampleDataRO(INDEX3(m_N0-1,k1,k2+1, m_N0,m_N1));
479                            const register double* f_111 = in.getSampleDataRO(INDEX3(m_N0-1,k1+1,k2+1, m_N0,m_N1));
480                            const register double* f_110 = in.getSampleDataRO(INDEX3(m_N0-1,k1+1,k2, m_N0,m_N1));
481                            const register double* f_011 = in.getSampleDataRO(INDEX3(m_N0-2,k1+1,k2+1, m_N0,m_N1));
482                            const register double* f_010 = in.getSampleDataRO(INDEX3(m_N0-2,k1+1,k2, m_N0,m_N1));
483                            const register double* f_100 = in.getSampleDataRO(INDEX3(m_N0-1,k1,k2, m_N0,m_N1));
484                            double* o = out.getSampleDataRW(m_faceOffset[1]+INDEX2(k1,k2,m_NE1));
485                            for (index_t i=0; i < numComp; ++i) {
486                                const double V0=((f_110[i]-f_100[i])*C6 + (f_111[i]-f_101[i])*C2) / h1;
487                                const double V1=((f_110[i]-f_100[i])*C2 + (f_111[i]-f_101[i])*C6) / h1;
488                                const double V2=((f_101[i]-f_100[i])*C6 + (f_111[i]-f_110[i])*C2) / h2;
489                                const double V3=((f_101[i]-f_100[i])*C2 + (f_111[i]-f_110[i])*C6) / h2;
490                                o[INDEX3(i,0,0,numComp,3)] = ((f_100[i]-f_000[i])*C5 + (f_111[i]-f_011[i])*C0 + (f_101[i]+f_110[i]-f_001[i]-f_010[i])*C1) / h0;
491                                o[INDEX3(i,1,0,numComp,3)] = V0;
492                                o[INDEX3(i,2,0,numComp,3)] = V2;
493                                o[INDEX3(i,0,1,numComp,3)] = ((f_110[i]-f_010[i])*C5 + (f_101[i]-f_001[i])*C0 + (f_100[i]+f_111[i]-f_000[i]-f_011[i])*C1) / h0;
494                                o[INDEX3(i,1,1,numComp,3)] = V0;
495                                o[INDEX3(i,2,1,numComp,3)] = V3;
496                                o[INDEX3(i,0,2,numComp,3)] = ((f_101[i]-f_001[i])*C5 + (f_110[i]-f_010[i])*C0 + (f_100[i]+f_111[i]-f_000[i]-f_011[i])*C1) / h0;
497                                o[INDEX3(i,1,2,numComp,3)] = V1;
498                                o[INDEX3(i,2,2,numComp,3)] = V2;
499                                o[INDEX3(i,0,3,numComp,3)] = ((f_111[i]-f_011[i])*C5 + (f_100[i]-f_000[i])*C0 + (f_101[i]+f_110[i]-f_001[i]-f_010[i])*C1) / h0;
500                                o[INDEX3(i,1,3,numComp,3)] = V1;
501                                o[INDEX3(i,2,3,numComp,3)] = V3;
502                            } /* end of component loop i */
503                        } /* end of k1 loop */
504                    } /* end of k2 loop */
505                } /* end of face 1 */
506                if (m_faceOffset[2] > -1) {
507    #pragma omp for nowait
508                    for (index_t k2=0; k2 < m_NE2; ++k2) {
509                        for (index_t k0=0; k0 < m_NE0; ++k0) {
510                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,0,k2, m_N0,m_N1));
511                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,0,k2+1, m_N0,m_N1));
512                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,0,k2+1, m_N0,m_N1));
513                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,0,k2, m_N0,m_N1));
514                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,1,k2+1, m_N0,m_N1));
515                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,1,k2, m_N0,m_N1));
516                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,1,k2+1, m_N0,m_N1));
517                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,1,k2, m_N0,m_N1));
518                            double* o = out.getSampleDataRW(m_faceOffset[2]+INDEX2(k0,k2,m_NE0));
519                            for (index_t i=0; i < numComp; ++i) {
520                                const double V0=((f_100[i]-f_000[i])*C6 + (f_101[i]-f_001[i])*C2) / h0;
521                                const double V1=((f_001[i]-f_000[i])*C6 + (f_101[i]-f_100[i])*C2) / h2;
522                                const double V2=((f_001[i]-f_000[i])*C2 + (f_101[i]-f_100[i])*C6) / h2;
523                                o[INDEX3(i,0,0,numComp,3)] = V0;
524                                o[INDEX3(i,1,0,numComp,3)] = ((f_010[i]-f_000[i])*C5 + (f_111[i]-f_101[i])*C0 + (f_011[i]+f_110[i]-f_001[i]-f_100[i])*C1) / h1;
525                                o[INDEX3(i,2,0,numComp,3)] = V1;
526                                o[INDEX3(i,0,1,numComp,3)] = V0;
527                                o[INDEX3(i,1,1,numComp,3)] = ((f_110[i]-f_100[i])*C5 + (f_011[i]-f_001[i])*C0 + (f_010[i]+f_111[i]-f_000[i]-f_101[i])*C1) / h1;
528                                o[INDEX3(i,2,1,numComp,3)] = V2;
529                                o[INDEX3(i,0,2,numComp,3)] = V0;
530                                o[INDEX3(i,1,2,numComp,3)] = ((f_011[i]-f_001[i])*C5 + (f_110[i]-f_100[i])*C0 + (f_010[i]+f_111[i]-f_000[i]-f_101[i])*C1) / h1;
531                                o[INDEX3(i,2,2,numComp,3)] = V1;
532                                o[INDEX3(i,0,3,numComp,3)] = V0;
533                                o[INDEX3(i,1,3,numComp,3)] = ((f_111[i]-f_101[i])*C5 + (f_010[i]-f_000[i])*C0 + (f_011[i]+f_110[i]-f_001[i]-f_100[i])*C1) / h1;
534                                o[INDEX3(i,2,3,numComp,3)] = V2;
535                            } /* end of component loop i */
536                        } /* end of k0 loop */
537                    } /* end of k2 loop */
538                } /* end of face 2 */
539                if (m_faceOffset[3] > -1) {
540    #pragma omp for nowait
541                    for (index_t k2=0; k2 < m_NE2; ++k2) {
542                        for (index_t k0=0; k0 < m_NE0; ++k0) {
543                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,m_N1-1,k2+1, m_N0,m_N1));
544                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,m_N1-1,k2, m_N0,m_N1));
545                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,m_N1-1,k2, m_N0,m_N1));
546                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,m_N1-1,k2+1, m_N0,m_N1));
547                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,m_N1-2,k2, m_N0,m_N1));
548                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,m_N1-2,k2+1, m_N0,m_N1));
549                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,m_N1-2,k2+1, m_N0,m_N1));
550                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,m_N1-2,k2, m_N0,m_N1));
551                            double* o = out.getSampleDataRW(m_faceOffset[3]+INDEX2(k0,k2,m_NE0));
552                            for (index_t i=0; i < numComp; ++i) {
553                                const double V0=((f_110[i]-f_010[i])*C6 + (f_111[i]-f_011[i])*C2) / h0;
554                                const double V1=((f_110[i]-f_010[i])*C2 + (f_111[i]-f_011[i])*C6) / h0;
555                                const double V2=((f_011[i]-f_010[i])*C6 + (f_111[i]-f_110[i])*C2) / h2;
556                                const double V3=((f_011[i]-f_010[i])*C2 + (f_111[i]-f_110[i])*C6) / h2;
557                                o[INDEX3(i,0,0,numComp,3)] = V0;
558                                o[INDEX3(i,1,0,numComp,3)] = ((f_010[i]-f_000[i])*C5 + (f_111[i]-f_101[i])*C0 + (f_011[i]+f_110[i]-f_001[i]-f_100[i])*C1) / h1;
559                                o[INDEX3(i,2,0,numComp,3)] = V2;
560                                o[INDEX3(i,0,1,numComp,3)] = V0;
561                                o[INDEX3(i,1,1,numComp,3)] = ((f_110[i]-f_100[i])*C5 + (f_011[i]-f_001[i])*C0 + (f_010[i]+f_111[i]-f_000[i]-f_101[i])*C1) / h1;
562                                o[INDEX3(i,2,1,numComp,3)] = V3;
563                                o[INDEX3(i,0,2,numComp,3)] = V1;
564                                o[INDEX3(i,1,2,numComp,3)] = ((f_011[i]-f_001[i])*C5 + (f_110[i]-f_100[i])*C0 + (f_010[i]+f_111[i]-f_000[i]-f_101[i])*C1) / h1;
565                                o[INDEX3(i,2,2,numComp,3)] = V2;
566                                o[INDEX3(i,0,3,numComp,3)] = V1;
567                                o[INDEX3(i,1,3,numComp,3)] = ((f_111[i]-f_101[i])*C5 + (f_010[i]-f_000[i])*C0 + (f_011[i]+f_110[i]-f_001[i]-f_100[i])*C1) / h1;
568                                o[INDEX3(i,2,3,numComp,3)] = V3;
569                            } /* end of component loop i */
570                        } /* end of k0 loop */
571                    } /* end of k2 loop */
572                } /* end of face 3 */
573                if (m_faceOffset[4] > -1) {
574    #pragma omp for nowait
575                    for (index_t k1=0; k1 < m_NE1; ++k1) {
576                        for (index_t k0=0; k0 < m_NE0; ++k0) {
577                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,0, m_N0,m_N1));
578                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,0, m_N0,m_N1));
579                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,0, m_N0,m_N1));
580                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,0, m_N0,m_N1));
581                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,1, m_N0,m_N1));
582                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,1, m_N0,m_N1));
583                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,1, m_N0,m_N1));
584                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,1, m_N0,m_N1));
585                            double* o = out.getSampleDataRW(m_faceOffset[4]+INDEX2(k0,k1,m_NE0));
586                            for (index_t i=0; i < numComp; ++i) {
587                                const double V0=((f_100[i]-f_000[i])*C6 + (f_110[i]-f_010[i])*C2) / h0;
588                                const double V1=((f_100[i]-f_000[i])*C2 + (f_110[i]-f_010[i])*C6) / h0;
589                                const double V2=((f_010[i]-f_000[i])*C6 + (f_110[i]-f_100[i])*C2) / h1;
590                                const double V3=((f_010[i]-f_000[i])*C2 + (f_110[i]-f_100[i])*C6) / h1;
591                                o[INDEX3(i,0,0,numComp,3)] = V0;
592                                o[INDEX3(i,1,0,numComp,3)] = V2;
593                                o[INDEX3(i,2,0,numComp,3)] = ((f_001[i]-f_000[i])*C5 + (f_111[i]-f_110[i])*C0 + (f_011[i]+f_101[i]-f_010[i]-f_100[i])*C1) / h2;
594                                o[INDEX3(i,0,1,numComp,3)] = V0;
595                                o[INDEX3(i,1,1,numComp,3)] = V3;
596                                o[INDEX3(i,2,1,numComp,3)] = ((f_101[i]-f_100[i])*C5 + (f_011[i]-f_010[i])*C0 + (f_001[i]+f_111[i]-f_000[i]-f_110[i])*C1) / h2;
597                                o[INDEX3(i,0,2,numComp,3)] = V1;
598                                o[INDEX3(i,1,2,numComp,3)] = V2;
599                                o[INDEX3(i,2,2,numComp,3)] = ((f_011[i]-f_010[i])*C5 + (f_101[i]-f_100[i])*C0 + (f_001[i]+f_111[i]-f_000[i]-f_110[i])*C1) / h2;
600                                o[INDEX3(i,0,3,numComp,3)] = V1;
601                                o[INDEX3(i,1,3,numComp,3)] = V3;
602                                o[INDEX3(i,2,3,numComp,3)] = ((f_111[i]-f_110[i])*C5 + (f_001[i]-f_000[i])*C0 + (f_011[i]+f_101[i]-f_010[i]-f_100[i])*C1) / h2;
603                            } /* end of component loop i */
604                        } /* end of k0 loop */
605                    } /* end of k1 loop */
606                } /* end of face 4 */
607                if (m_faceOffset[5] > -1) {
608    #pragma omp for nowait
609                    for (index_t k1=0; k1 < m_NE1; ++k1) {
610                        for (index_t k0=0; k0 < m_NE0; ++k0) {
611                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,m_N2-1, m_N0,m_N1));
612                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,m_N2-1, m_N0,m_N1));
613                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,m_N2-1, m_N0,m_N1));
614                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,m_N2-1, m_N0,m_N1));
615                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,m_N2-2, m_N0,m_N1));
616                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,m_N2-2, m_N0,m_N1));
617                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,m_N2-2, m_N0,m_N1));
618                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,m_N2-2, m_N0,m_N1));
619                            double* o = out.getSampleDataRW(m_faceOffset[5]+INDEX2(k0,k1,m_NE0));
620                            for (index_t i=0; i < numComp; ++i) {
621                                const double V0=((f_101[i]-f_001[i])*C6 + (f_111[i]-f_011[i])*C2) / h0;
622                                const double V1=((f_101[i]-f_001[i])*C2 + (f_111[i]-f_011[i])*C6) / h0;
623                                const double V2=((f_011[i]-f_001[i])*C6 + (f_111[i]-f_101[i])*C2) / h1;
624                                const double V3=((f_011[i]-f_001[i])*C2 + (f_111[i]-f_101[i])*C6) / h1;
625                                o[INDEX3(i,0,0,numComp,3)] = V0;
626                                o[INDEX3(i,1,0,numComp,3)] = V2;
627                                o[INDEX3(i,2,0,numComp,3)] = ((f_001[i]-f_000[i])*C5 + (f_111[i]-f_110[i])*C0 + (f_011[i]+f_101[i]-f_010[i]-f_100[i])*C1) / h2;
628                                o[INDEX3(i,0,1,numComp,3)] = V0;
629                                o[INDEX3(i,1,1,numComp,3)] = V3;
630                                o[INDEX3(i,2,1,numComp,3)] = ((f_011[i]-f_010[i])*C0 + (f_101[i]-f_100[i])*C5 + (f_001[i]+f_111[i]-f_000[i]-f_110[i])*C1) / h2;
631                                o[INDEX3(i,0,2,numComp,3)] = V1;
632                                o[INDEX3(i,1,2,numComp,3)] = V2;
633                                o[INDEX3(i,2,2,numComp,3)] = ((f_011[i]-f_010[i])*C5 + (f_101[i]-f_100[i])*C0 + (f_001[i]+f_111[i]-f_000[i]-f_110[i])*C1) / h2;
634                                o[INDEX3(i,0,3,numComp,3)] = V1;
635                                o[INDEX3(i,1,3,numComp,3)] = V3;
636                                o[INDEX3(i,2,3,numComp,3)] = ((f_001[i]-f_000[i])*C0 + (f_111[i]-f_110[i])*C5 + (f_011[i]+f_101[i]-f_010[i]-f_100[i])*C1) / h2;
637                            } /* end of component loop i */
638                        } /* end of k0 loop */
639                    } /* end of k1 loop */
640                } /* end of face 5 */
641            } // end of parallel section
642            /* GENERATOR SNIP_GRAD_FACES BOTTOM */
643        } else if (out.getFunctionSpace().getTypeCode() == ReducedFaceElements) {
644            out.requireWrite();
645            /*** GENERATOR SNIP_GRAD_REDUCED_FACES TOP */
646    #pragma omp parallel
647            {
648                if (m_faceOffset[0] > -1) {
649    #pragma omp for nowait
650                    for (index_t k2=0; k2 < m_NE2; ++k2) {
651                        for (index_t k1=0; k1 < m_NE1; ++k1) {
652                            const register double* f_000 = in.getSampleDataRO(INDEX3(0,k1,k2, m_N0,m_N1));
653                            const register double* f_001 = in.getSampleDataRO(INDEX3(0,k1,k2+1, m_N0,m_N1));
654                            const register double* f_101 = in.getSampleDataRO(INDEX3(1,k1,k2+1, m_N0,m_N1));
655                            const register double* f_011 = in.getSampleDataRO(INDEX3(0,k1+1,k2+1, m_N0,m_N1));
656                            const register double* f_100 = in.getSampleDataRO(INDEX3(1,k1,k2, m_N0,m_N1));
657                            const register double* f_110 = in.getSampleDataRO(INDEX3(1,k1+1,k2, m_N0,m_N1));
658                            const register double* f_010 = in.getSampleDataRO(INDEX3(0,k1+1,k2, m_N0,m_N1));
659                            const register double* f_111 = in.getSampleDataRO(INDEX3(1,k1+1,k2+1, m_N0,m_N1));
660                            double* o = out.getSampleDataRW(m_faceOffset[0]+INDEX2(k1,k2,m_NE1));
661                            for (index_t i=0; i < numComp; ++i) {
662                                o[INDEX3(i,0,0,numComp,3)] = (f_100[i]+f_101[i]+f_110[i]+f_111[i]-f_000[i]-f_001[i]-f_010[i]-f_011[i])*C3 / h0;
663                                o[INDEX3(i,1,0,numComp,3)] = (f_010[i]+f_011[i]-f_000[i]-f_001[i])*C4 / h1;
664                                o[INDEX3(i,2,0,numComp,3)] = (f_001[i]+f_011[i]-f_000[i]-f_010[i])*C4 / h2;
665                            } /* end of component loop i */
666                        } /* end of k1 loop */
667                    } /* end of k2 loop */
668                } /* end of face 0 */
669                if (m_faceOffset[1] > -1) {
670    #pragma omp for nowait
671                    for (index_t k2=0; k2 < m_NE2; ++k2) {
672                        for (index_t k1=0; k1 < m_NE1; ++k1) {
673                            const register double* f_000 = in.getSampleDataRO(INDEX3(m_N0-2,k1,k2, m_N0,m_N1));
674                            const register double* f_001 = in.getSampleDataRO(INDEX3(m_N0-2,k1,k2+1, m_N0,m_N1));
675                            const register double* f_101 = in.getSampleDataRO(INDEX3(m_N0-1,k1,k2+1, m_N0,m_N1));
676                            const register double* f_011 = in.getSampleDataRO(INDEX3(m_N0-2,k1+1,k2+1, m_N0,m_N1));
677                            const register double* f_100 = in.getSampleDataRO(INDEX3(m_N0-1,k1,k2, m_N0,m_N1));
678                            const register double* f_110 = in.getSampleDataRO(INDEX3(m_N0-1,k1+1,k2, m_N0,m_N1));
679                            const register double* f_010 = in.getSampleDataRO(INDEX3(m_N0-2,k1+1,k2, m_N0,m_N1));
680                            const register double* f_111 = in.getSampleDataRO(INDEX3(m_N0-1,k1+1,k2+1, m_N0,m_N1));
681                            double* o = out.getSampleDataRW(m_faceOffset[1]+INDEX2(k1,k2,m_NE1));
682                            for (index_t i=0; i < numComp; ++i) {
683                                o[INDEX3(i,0,0,numComp,3)] = (f_100[i]+f_101[i]+f_110[i]+f_111[i]-f_000[i]-f_001[i]-f_010[i]-f_011[i])*C3 / h0;
684                                o[INDEX3(i,1,0,numComp,3)] = (f_110[i]+f_111[i]-f_100[i]-f_101[i])*C4 / h1;
685                                o[INDEX3(i,2,0,numComp,3)] = (f_101[i]+f_111[i]-f_100[i]-f_110[i])*C4 / h2;
686                            } /* end of component loop i */
687                        } /* end of k1 loop */
688                    } /* end of k2 loop */
689                } /* end of face 1 */
690                if (m_faceOffset[2] > -1) {
691    #pragma omp for nowait
692                    for (index_t k2=0; k2 < m_NE2; ++k2) {
693                        for (index_t k0=0; k0 < m_NE0; ++k0) {
694                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,0,k2, m_N0,m_N1));
695                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,0,k2+1, m_N0,m_N1));
696                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,0,k2+1, m_N0,m_N1));
697                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,0,k2, m_N0,m_N1));
698                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,1,k2+1, m_N0,m_N1));
699                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,1,k2, m_N0,m_N1));
700                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,1,k2, m_N0,m_N1));
701                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,1,k2+1, m_N0,m_N1));
702                            double* o = out.getSampleDataRW(m_faceOffset[2]+INDEX2(k0,k2,m_NE0));
703                            for (index_t i=0; i < numComp; ++i) {
704                                o[INDEX3(i,0,0,numComp,3)] = (f_100[i]+f_101[i]-f_000[i]-f_001[i])*C4 / h0;
705                                o[INDEX3(i,1,0,numComp,3)] = (f_010[i]+f_011[i]+f_110[i]+f_111[i]-f_000[i]-f_001[i]-f_100[i]-f_101[i])*C3 / h1;
706                                o[INDEX3(i,2,0,numComp,3)] = (f_001[i]+f_101[i]-f_000[i]-f_100[i])*C4 / h2;
707                            } /* end of component loop i */
708                        } /* end of k0 loop */
709                    } /* end of k2 loop */
710                } /* end of face 2 */
711                if (m_faceOffset[3] > -1) {
712    #pragma omp for nowait
713                    for (index_t k2=0; k2 < m_NE2; ++k2) {
714                        for (index_t k0=0; k0 < m_NE0; ++k0) {
715                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,m_N1-1,k2+1, m_N0,m_N1));
716                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,m_N1-1,k2, m_N0,m_N1));
717                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,m_N1-1,k2, m_N0,m_N1));
718                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,m_N1-1,k2+1, m_N0,m_N1));
719                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,m_N1-2,k2, m_N0,m_N1));
720                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,m_N1-2,k2+1, m_N0,m_N1));
721                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,m_N1-2,k2+1, m_N0,m_N1));
722                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,m_N1-2,k2, m_N0,m_N1));
723                            double* o = out.getSampleDataRW(m_faceOffset[3]+INDEX2(k0,k2,m_NE0));
724                            for (index_t i=0; i < numComp; ++i) {
725                                o[INDEX3(i,0,0,numComp,3)] = (f_110[i]+f_111[i]-f_010[i]-f_011[i])*C4 / h0;
726                                o[INDEX3(i,1,0,numComp,3)] = (f_010[i]+f_011[i]+f_110[i]+f_111[i]-f_000[i]-f_001[i]-f_100[i]-f_101[i])*C3 / h1;
727                                o[INDEX3(i,2,0,numComp,3)] = (f_011[i]+f_111[i]-f_010[i]-f_110[i])*C4 / h2;
728                            } /* end of component loop i */
729                        } /* end of k0 loop */
730                    } /* end of k2 loop */
731                } /* end of face 3 */
732                if (m_faceOffset[4] > -1) {
733    #pragma omp for nowait
734                    for (index_t k1=0; k1 < m_NE1; ++k1) {
735                        for (index_t k0=0; k0 < m_NE0; ++k0) {
736                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,0, m_N0,m_N1));
737                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,0, m_N0,m_N1));
738                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,0, m_N0,m_N1));
739                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,0, m_N0,m_N1));
740                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,1, m_N0,m_N1));
741                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,1, m_N0,m_N1));
742                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,1, m_N0,m_N1));
743                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,1, m_N0,m_N1));
744                            double* o = out.getSampleDataRW(m_faceOffset[4]+INDEX2(k0,k1,m_NE0));
745                            for (index_t i=0; i < numComp; ++i) {
746                                o[INDEX3(i,0,0,numComp,3)] = (f_100[i]+f_110[i]-f_000[i]-f_010[i])*C4 / h0;
747                                o[INDEX3(i,1,0,numComp,3)] = (f_010[i]+f_110[i]-f_000[i]-f_100[i])*C4 / h1;
748                                o[INDEX3(i,2,0,numComp,3)] = (f_001[i]+f_011[i]+f_101[i]+f_111[i]-f_000[i]-f_010[i]-f_100[i]-f_110[i])*C4 / h2;
749                            } /* end of component loop i */
750                        } /* end of k0 loop */
751                    } /* end of k1 loop */
752                } /* end of face 4 */
753                if (m_faceOffset[5] > -1) {
754    #pragma omp for nowait
755                    for (index_t k1=0; k1 < m_NE1; ++k1) {
756                        for (index_t k0=0; k0 < m_NE0; ++k0) {
757                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,m_N2-1, m_N0,m_N1));
758                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,m_N2-1, m_N0,m_N1));
759                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,m_N2-1, m_N0,m_N1));
760                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,m_N2-1, m_N0,m_N1));
761                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,m_N2-2, m_N0,m_N1));
762                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,m_N2-2, m_N0,m_N1));
763                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,m_N2-2, m_N0,m_N1));
764                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,m_N2-2, m_N0,m_N1));
765                            double* o = out.getSampleDataRW(m_faceOffset[5]+INDEX2(k0,k1,m_NE0));
766                            for (index_t i=0; i < numComp; ++i) {
767                                o[INDEX3(i,0,0,numComp,3)] = (f_101[i]+f_111[i]-f_001[i]-f_011[i])*C4 / h0;
768                                o[INDEX3(i,1,0,numComp,3)] = (f_011[i]+f_111[i]-f_001[i]-f_101[i])*C4 / h1;
769                                o[INDEX3(i,2,0,numComp,3)] = (f_001[i]+f_011[i]+f_101[i]+f_111[i]-f_000[i]-f_010[i]-f_100[i]-f_110[i])*C3 / h2;
770                            } /* end of component loop i */
771                        } /* end of k0 loop */
772                    } /* end of k1 loop */
773                } /* end of face 5 */
774            } // end of parallel section
775            /* GENERATOR SNIP_GRAD_REDUCED_FACES BOTTOM */
776        } else {
777            stringstream msg;
778            msg << "setToGradient() not implemented for "
779                << functionSpaceTypeAsString(out.getFunctionSpace().getTypeCode());
780            throw RipleyException(msg.str());
781        }
782    }
783    
784    void Brick::setToIntegrals(vector<double>& integrals, const escript::Data& arg) const
785    {
786        escript::Data& in = *const_cast<escript::Data*>(&arg);
787        const dim_t numComp = in.getDataPointSize();
788        const double h0 = m_l0/m_gNE0;
789        const double h1 = m_l1/m_gNE1;
790        const double h2 = m_l2/m_gNE2;
791        if (arg.getFunctionSpace().getTypeCode() == Elements) {
792            const double w_0 = h0*h1*h2/8.;
793    #pragma omp parallel
794            {
795                vector<double> int_local(numComp, 0);
796    #pragma omp for nowait
797                for (index_t k2 = 0; k2 < m_NE2; ++k2) {
798                    for (index_t k1 = 0; k1 < m_NE1; ++k1) {
799                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
800                            const double* f = in.getSampleDataRO(INDEX3(k0, k1, k2, m_NE0, m_NE1));
801                            for (index_t i=0; i < numComp; ++i) {
802                                const register double f_0 = f[INDEX2(i,0,numComp)];
803                                const register double f_1 = f[INDEX2(i,1,numComp)];
804                                const register double f_2 = f[INDEX2(i,2,numComp)];
805                                const register double f_3 = f[INDEX2(i,3,numComp)];
806                                const register double f_4 = f[INDEX2(i,4,numComp)];
807                                const register double f_5 = f[INDEX2(i,5,numComp)];
808                                const register double f_6 = f[INDEX2(i,6,numComp)];
809                                const register double f_7 = f[INDEX2(i,7,numComp)];
810                                int_local[i]+=(f_0+f_1+f_2+f_3+f_4+f_5+f_6+f_7)*w_0;
811                            }  /* end of component loop i */
812                        } /* end of k0 loop */
813                    } /* end of k1 loop */
814                } /* end of k2 loop */
815    
816    #pragma omp critical
817                for (index_t i=0; i<numComp; i++)
818                    integrals[i]+=int_local[i];
819            } // end of parallel section
820        } else if (arg.getFunctionSpace().getTypeCode() == ReducedElements) {
821            const double w_0 = h0*h1*h2;
822    #pragma omp parallel
823            {
824                vector<double> int_local(numComp, 0);
825    #pragma omp for nowait
826                for (index_t k2 = 0; k2 < m_NE2; ++k2) {
827                    for (index_t k1 = 0; k1 < m_NE1; ++k1) {
828                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
829                            const double* f = in.getSampleDataRO(INDEX3(k0, k1, k2, m_NE0, m_NE1));
830                            for (index_t i=0; i < numComp; ++i) {
831                                int_local[i]+=f[i]*w_0;
832                            }  /* end of component loop i */
833                        } /* end of k0 loop */
834                    } /* end of k1 loop */
835                } /* end of k2 loop */
836    
837    #pragma omp critical
838                for (index_t i=0; i<numComp; i++)
839                    integrals[i]+=int_local[i];
840            } // end of parallel section
841        } else if (arg.getFunctionSpace().getTypeCode() == FaceElements) {
842            const double w_0 = h1*h2/4.;
843            const double w_1 = h0*h2/4.;
844            const double w_2 = h0*h1/4.;
845    #pragma omp parallel
846            {
847                vector<double> int_local(numComp, 0);
848                if (m_faceOffset[0] > -1) {
849    #pragma omp for nowait
850                    for (index_t k2=0; k2 < m_NE2; ++k2) {
851                        for (index_t k1=0; k1 < m_NE1; ++k1) {
852                            const double* f = in.getSampleDataRO(m_faceOffset[0]+INDEX2(k1,k2,m_NE1));
853                            for (index_t i=0; i < numComp; ++i) {
854                                const register double f_0 = f[INDEX2(i,0,numComp)];
855                                const register double f_1 = f[INDEX2(i,1,numComp)];
856                                const register double f_2 = f[INDEX2(i,2,numComp)];
857                                const register double f_3 = f[INDEX2(i,3,numComp)];
858                                int_local[i]+=(f_0+f_1+f_2+f_3)*w_0;
859                            }  /* end of component loop i */
860                        } /* end of k1 loop */
861                    } /* end of k2 loop */
862                }
863    
864                if (m_faceOffset[1] > -1) {
865    #pragma omp for nowait
866                    for (index_t k2=0; k2 < m_NE2; ++k2) {
867                        for (index_t k1=0; k1 < m_NE1; ++k1) {
868                            const double* f = in.getSampleDataRO(m_faceOffset[1]+INDEX2(k1,k2,m_NE1));
869                            for (index_t i=0; i < numComp; ++i) {
870                                const register double f_0 = f[INDEX2(i,0,numComp)];
871                                const register double f_1 = f[INDEX2(i,1,numComp)];
872                                const register double f_2 = f[INDEX2(i,2,numComp)];
873                                const register double f_3 = f[INDEX2(i,3,numComp)];
874                                int_local[i]+=(f_0+f_1+f_2+f_3)*w_0;
875                            }  /* end of component loop i */
876                        } /* end of k1 loop */
877                    } /* end of k2 loop */
878                }
879    
880                if (m_faceOffset[2] > -1) {
881    #pragma omp for nowait
882                    for (index_t k2=0; k2 < m_NE2; ++k2) {
883                        for (index_t k0=0; k0 < m_NE0; ++k0) {
884                            const double* f = in.getSampleDataRO(m_faceOffset[2]+INDEX2(k0,k2,m_NE0));
885                            for (index_t i=0; i < numComp; ++i) {
886                                const register double f_0 = f[INDEX2(i,0,numComp)];
887                                const register double f_1 = f[INDEX2(i,1,numComp)];
888                                const register double f_2 = f[INDEX2(i,2,numComp)];
889                                const register double f_3 = f[INDEX2(i,3,numComp)];
890                                int_local[i]+=(f_0+f_1+f_2+f_3)*w_1;
891                            }  /* end of component loop i */
892                        } /* end of k1 loop */
893                    } /* end of k2 loop */
894                }
895    
896                if (m_faceOffset[3] > -1) {
897    #pragma omp for nowait
898                    for (index_t k2=0; k2 < m_NE2; ++k2) {
899                        for (index_t k0=0; k0 < m_NE0; ++k0) {
900                            const double* f = in.getSampleDataRO(m_faceOffset[3]+INDEX2(k0,k2,m_NE0));
901                            for (index_t i=0; i < numComp; ++i) {
902                                const register double f_0 = f[INDEX2(i,0,numComp)];
903                                const register double f_1 = f[INDEX2(i,1,numComp)];
904                                const register double f_2 = f[INDEX2(i,2,numComp)];
905                                const register double f_3 = f[INDEX2(i,3,numComp)];
906                                int_local[i]+=(f_0+f_1+f_2+f_3)*w_1;
907                            }  /* end of component loop i */
908                        } /* end of k1 loop */
909                    } /* end of k2 loop */
910                }
911    
912                if (m_faceOffset[4] > -1) {
913    #pragma omp for nowait
914                    for (index_t k1=0; k1 < m_NE1; ++k1) {
915                        for (index_t k0=0; k0 < m_NE0; ++k0) {
916                            const double* f = in.getSampleDataRO(m_faceOffset[4]+INDEX2(k0,k1,m_NE0));
917                            for (index_t i=0; i < numComp; ++i) {
918                                const register double f_0 = f[INDEX2(i,0,numComp)];
919                                const register double f_1 = f[INDEX2(i,1,numComp)];
920                                const register double f_2 = f[INDEX2(i,2,numComp)];
921                                const register double f_3 = f[INDEX2(i,3,numComp)];
922                                int_local[i]+=(f_0+f_1+f_2+f_3)*w_2;
923                            }  /* end of component loop i */
924                        } /* end of k1 loop */
925                    } /* end of k2 loop */
926                }
927    
928                if (m_faceOffset[5] > -1) {
929    #pragma omp for nowait
930                    for (index_t k1=0; k1 < m_NE1; ++k1) {
931                        for (index_t k0=0; k0 < m_NE0; ++k0) {
932                            const double* f = in.getSampleDataRO(m_faceOffset[5]+INDEX2(k0,k1,m_NE0));
933                            for (index_t i=0; i < numComp; ++i) {
934                                const register double f_0 = f[INDEX2(i,0,numComp)];
935                                const register double f_1 = f[INDEX2(i,1,numComp)];
936                                const register double f_2 = f[INDEX2(i,2,numComp)];
937                                const register double f_3 = f[INDEX2(i,3,numComp)];
938                                int_local[i]+=(f_0+f_1+f_2+f_3)*w_2;
939                            }  /* end of component loop i */
940                        } /* end of k1 loop */
941                    } /* end of k2 loop */
942                }
943    
944    #pragma omp critical
945                for (index_t i=0; i<numComp; i++)
946                    integrals[i]+=int_local[i];
947            } // end of parallel section
948    
949        } else if (arg.getFunctionSpace().getTypeCode() == ReducedFaceElements) {
950            const double w_0 = h1*h2;
951            const double w_1 = h0*h2;
952            const double w_2 = h0*h1;
953    #pragma omp parallel
954            {
955                vector<double> int_local(numComp, 0);
956                if (m_faceOffset[0] > -1) {
957    #pragma omp for nowait
958                    for (index_t k2=0; k2 < m_NE2; ++k2) {
959                        for (index_t k1=0; k1 < m_NE1; ++k1) {
960                            const double* f = in.getSampleDataRO(m_faceOffset[0]+INDEX2(k1,k2,m_NE1));
961                            for (index_t i=0; i < numComp; ++i) {
962                                int_local[i]+=f[i]*w_0;
963                            }  /* end of component loop i */
964                        } /* end of k1 loop */
965                    } /* end of k2 loop */
966                }
967    
968                if (m_faceOffset[1] > -1) {
969    #pragma omp for nowait
970                    for (index_t k2=0; k2 < m_NE2; ++k2) {
971                        for (index_t k1=0; k1 < m_NE1; ++k1) {
972                            const double* f = in.getSampleDataRO(m_faceOffset[1]+INDEX2(k1,k2,m_NE1));
973                            for (index_t i=0; i < numComp; ++i) {
974                                int_local[i]+=f[i]*w_0;
975                            }  /* end of component loop i */
976                        } /* end of k1 loop */
977                    } /* end of k2 loop */
978                }
979    
980                if (m_faceOffset[2] > -1) {
981    #pragma omp for nowait
982                    for (index_t k2=0; k2 < m_NE2; ++k2) {
983                        for (index_t k0=0; k0 < m_NE0; ++k0) {
984                            const double* f = in.getSampleDataRO(m_faceOffset[2]+INDEX2(k0,k2,m_NE0));
985                            for (index_t i=0; i < numComp; ++i) {
986                                int_local[i]+=f[i]*w_1;
987                            }  /* end of component loop i */
988                        } /* end of k1 loop */
989                    } /* end of k2 loop */
990                }
991    
992                if (m_faceOffset[3] > -1) {
993    #pragma omp for nowait
994                    for (index_t k2=0; k2 < m_NE2; ++k2) {
995                        for (index_t k0=0; k0 < m_NE0; ++k0) {
996                            const double* f = in.getSampleDataRO(m_faceOffset[3]+INDEX2(k0,k2,m_NE0));
997                            for (index_t i=0; i < numComp; ++i) {
998                                int_local[i]+=f[i]*w_1;
999                            }  /* end of component loop i */
1000                        } /* end of k1 loop */
1001                    } /* end of k2 loop */
1002                }
1003    
1004                if (m_faceOffset[4] > -1) {
1005    #pragma omp for nowait
1006                    for (index_t k1=0; k1 < m_NE1; ++k1) {
1007                        for (index_t k0=0; k0 < m_NE0; ++k0) {
1008                            const double* f = in.getSampleDataRO(m_faceOffset[4]+INDEX2(k0,k1,m_NE0));
1009                            for (index_t i=0; i < numComp; ++i) {
1010                                int_local[i]+=f[i]*w_2;
1011                            }  /* end of component loop i */
1012                        } /* end of k1 loop */
1013                    } /* end of k2 loop */
1014                }
1015    
1016                if (m_faceOffset[5] > -1) {
1017    #pragma omp for nowait
1018                    for (index_t k1=0; k1 < m_NE1; ++k1) {
1019                        for (index_t k0=0; k0 < m_NE0; ++k0) {
1020                            const double* f = in.getSampleDataRO(m_faceOffset[5]+INDEX2(k0,k1,m_NE0));
1021                            for (index_t i=0; i < numComp; ++i) {
1022                                int_local[i]+=f[i]*w_2;
1023                            }  /* end of component loop i */
1024                        } /* end of k1 loop */
1025                    } /* end of k2 loop */
1026                }
1027    
1028    #pragma omp critical
1029                for (index_t i=0; i<numComp; i++)
1030                    integrals[i]+=int_local[i];
1031            } // end of parallel section
1032    
1033      } else {      } else {
1034          throw RipleyException("setToGradient() not implemented");          stringstream msg;
1035            msg << "setToIntegrals() not implemented for "
1036                << functionSpaceTypeAsString(arg.getFunctionSpace().getTypeCode());
1037            throw RipleyException(msg.str());
1038        }
1039    }
1040    
1041    void Brick::setToNormal(escript::Data& out) const
1042    {
1043        if (out.getFunctionSpace().getTypeCode() == FaceElements) {
1044            out.requireWrite();
1045    #pragma omp parallel
1046            {
1047                if (m_faceOffset[0] > -1) {
1048    #pragma omp for nowait
1049                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1050                        for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1051                            double* o = out.getSampleDataRW(m_faceOffset[0]+INDEX2(k1,k2,m_NE1));
1052                            // set vector at four quadrature points
1053                            *o++ = -1.; *o++ = 0.; *o++ = 0.;
1054                            *o++ = -1.; *o++ = 0.; *o++ = 0.;
1055                            *o++ = -1.; *o++ = 0.; *o++ = 0.;
1056                            *o++ = -1.; *o++ = 0.; *o = 0.;
1057                        }
1058                    }
1059                }
1060    
1061                if (m_faceOffset[1] > -1) {
1062    #pragma omp for nowait
1063                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1064                        for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1065                            double* o = out.getSampleDataRW(m_faceOffset[1]+INDEX2(k1,k2,m_NE1));
1066                            // set vector at four quadrature points
1067                            *o++ = 1.; *o++ = 0.; *o++ = 0.;
1068                            *o++ = 1.; *o++ = 0.; *o++ = 0.;
1069                            *o++ = 1.; *o++ = 0.; *o++ = 0.;
1070                            *o++ = 1.; *o++ = 0.; *o = 0.;
1071                        }
1072                    }
1073                }
1074    
1075                if (m_faceOffset[2] > -1) {
1076    #pragma omp for nowait
1077                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1078                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1079                            double* o = out.getSampleDataRW(m_faceOffset[2]+INDEX2(k0,k2,m_NE0));
1080                            // set vector at four quadrature points
1081                            *o++ = 0.; *o++ = -1.; *o++ = 0.;
1082                            *o++ = 0.; *o++ = -1.; *o++ = 0.;
1083                            *o++ = 0.; *o++ = -1.; *o++ = 0.;
1084                            *o++ = 0.; *o++ = -1.; *o = 0.;
1085                        }
1086                    }
1087                }
1088    
1089                if (m_faceOffset[3] > -1) {
1090    #pragma omp for nowait
1091                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1092                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1093                            double* o = out.getSampleDataRW(m_faceOffset[3]+INDEX2(k0,k2,m_NE0));
1094                            // set vector at four quadrature points
1095                            *o++ = 0.; *o++ = 1.; *o++ = 0.;
1096                            *o++ = 0.; *o++ = 1.; *o++ = 0.;
1097                            *o++ = 0.; *o++ = 1.; *o++ = 0.;
1098                            *o++ = 0.; *o++ = 1.; *o = 0.;
1099                        }
1100                    }
1101                }
1102    
1103                if (m_faceOffset[4] > -1) {
1104    #pragma omp for nowait
1105                    for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1106                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1107                            double* o = out.getSampleDataRW(m_faceOffset[4]+INDEX2(k0,k1,m_NE0));
1108                            // set vector at four quadrature points
1109                            *o++ = 0.; *o++ = 0.; *o++ = -1.;
1110                            *o++ = 0.; *o++ = 0.; *o++ = -1.;
1111                            *o++ = 0.; *o++ = 0.; *o++ = -1.;
1112                            *o++ = 0.; *o++ = 0.; *o = -1.;
1113                        }
1114                    }
1115                }
1116    
1117                if (m_faceOffset[5] > -1) {
1118    #pragma omp for nowait
1119                    for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1120                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1121                            double* o = out.getSampleDataRW(m_faceOffset[5]+INDEX2(k0,k1,m_NE0));
1122                            // set vector at four quadrature points
1123                            *o++ = 0.; *o++ = 0.; *o++ = 1.;
1124                            *o++ = 0.; *o++ = 0.; *o++ = 1.;
1125                            *o++ = 0.; *o++ = 0.; *o++ = 1.;
1126                            *o++ = 0.; *o++ = 0.; *o = 1.;
1127                        }
1128                    }
1129                }
1130            } // end of parallel section
1131        } else if (out.getFunctionSpace().getTypeCode() == ReducedFaceElements) {
1132            out.requireWrite();
1133    #pragma omp parallel
1134            {
1135                if (m_faceOffset[0] > -1) {
1136    #pragma omp for nowait
1137                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1138                        for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1139                            double* o = out.getSampleDataRW(m_faceOffset[0]+INDEX2(k1,k2,m_NE1));
1140                            *o++ = -1.;
1141                            *o++ = 0.;
1142                            *o = 0.;
1143                        }
1144                    }
1145                }
1146    
1147                if (m_faceOffset[1] > -1) {
1148    #pragma omp for nowait
1149                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1150                        for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1151                            double* o = out.getSampleDataRW(m_faceOffset[1]+INDEX2(k1,k2,m_NE1));
1152                            *o++ = 1.;
1153                            *o++ = 0.;
1154                            *o = 0.;
1155                        }
1156                    }
1157                }
1158    
1159                if (m_faceOffset[2] > -1) {
1160    #pragma omp for nowait
1161                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1162                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1163                            double* o = out.getSampleDataRW(m_faceOffset[2]+INDEX2(k0,k2,m_NE0));
1164                            *o++ = 0.;
1165                            *o++ = -1.;
1166                            *o = 0.;
1167                        }
1168                    }
1169                }
1170    
1171                if (m_faceOffset[3] > -1) {
1172    #pragma omp for nowait
1173                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1174                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1175                            double* o = out.getSampleDataRW(m_faceOffset[3]+INDEX2(k0,k2,m_NE0));
1176                            *o++ = 0.;
1177                            *o++ = 1.;
1178                            *o = 0.;
1179                        }
1180                    }
1181                }
1182    
1183                if (m_faceOffset[4] > -1) {
1184    #pragma omp for nowait
1185                    for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1186                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1187                            double* o = out.getSampleDataRW(m_faceOffset[4]+INDEX2(k0,k1,m_NE0));
1188                            *o++ = 0.;
1189                            *o++ = 0.;
1190                            *o = -1.;
1191                        }
1192                    }
1193                }
1194    
1195                if (m_faceOffset[5] > -1) {
1196    #pragma omp for nowait
1197                    for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1198                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1199                            double* o = out.getSampleDataRW(m_faceOffset[5]+INDEX2(k0,k1,m_NE0));
1200                            *o++ = 0.;
1201                            *o++ = 0.;
1202                            *o = 1.;
1203                        }
1204                    }
1205                }
1206            } // end of parallel section
1207    
1208        } else {
1209            stringstream msg;
1210            msg << "setToNormal() not implemented for "
1211                << functionSpaceTypeAsString(out.getFunctionSpace().getTypeCode());
1212            throw RipleyException(msg.str());
1213        }
1214    }
1215    
1216    void Brick::setToSize(escript::Data& out) const
1217    {
1218        if (out.getFunctionSpace().getTypeCode() == Elements
1219                || out.getFunctionSpace().getTypeCode() == ReducedElements) {
1220            out.requireWrite();
1221            const dim_t numQuad=out.getNumDataPointsPerSample();
1222            const double xSize=getFirstCoordAndSpacing(0).second;
1223            const double ySize=getFirstCoordAndSpacing(1).second;
1224            const double zSize=getFirstCoordAndSpacing(2).second;
1225            const double size=min(min(xSize,ySize),zSize);
1226    #pragma omp parallel for
1227            for (index_t k = 0; k < getNumElements(); ++k) {
1228                double* o = out.getSampleDataRW(k);
1229                fill(o, o+numQuad, size);
1230            }
1231        } else if (out.getFunctionSpace().getTypeCode() == FaceElements
1232                || out.getFunctionSpace().getTypeCode() == ReducedFaceElements) {
1233            out.requireWrite();
1234            const dim_t numQuad=out.getNumDataPointsPerSample();
1235            const double xSize=getFirstCoordAndSpacing(0).second;
1236            const double ySize=getFirstCoordAndSpacing(1).second;
1237            const double zSize=getFirstCoordAndSpacing(2).second;
1238    #pragma omp parallel
1239            {
1240                if (m_faceOffset[0] > -1) {
1241                    const double size=min(ySize,zSize);
1242    #pragma omp for nowait
1243                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1244                        for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1245                            double* o = out.getSampleDataRW(m_faceOffset[0]+INDEX2(k1,k2,m_NE1));
1246                            fill(o, o+numQuad, size);
1247                        }
1248                    }
1249                }
1250    
1251                if (m_faceOffset[1] > -1) {
1252                    const double size=min(ySize,zSize);
1253    #pragma omp for nowait
1254                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1255                        for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1256                            double* o = out.getSampleDataRW(m_faceOffset[1]+INDEX2(k1,k2,m_NE1));
1257                            fill(o, o+numQuad, size);
1258                        }
1259                    }
1260                }
1261    
1262                if (m_faceOffset[2] > -1) {
1263                    const double size=min(xSize,zSize);
1264    #pragma omp for nowait
1265                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1266                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1267                            double* o = out.getSampleDataRW(m_faceOffset[2]+INDEX2(k0,k2,m_NE0));
1268                            fill(o, o+numQuad, size);
1269                        }
1270                    }
1271                }
1272    
1273                if (m_faceOffset[3] > -1) {
1274                    const double size=min(xSize,zSize);
1275    #pragma omp for nowait
1276                    for (index_t k2 = 0; k2 < m_NE2; ++k2) {
1277                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1278                            double* o = out.getSampleDataRW(m_faceOffset[3]+INDEX2(k0,k2,m_NE0));
1279                            fill(o, o+numQuad, size);
1280                        }
1281                    }
1282                }
1283    
1284                if (m_faceOffset[4] > -1) {
1285                    const double size=min(xSize,ySize);
1286    #pragma omp for nowait
1287                    for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1288                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1289                            double* o = out.getSampleDataRW(m_faceOffset[4]+INDEX2(k0,k1,m_NE0));
1290                            fill(o, o+numQuad, size);
1291                        }
1292                    }
1293                }
1294    
1295                if (m_faceOffset[5] > -1) {
1296                    const double size=min(xSize,ySize);
1297    #pragma omp for nowait
1298                    for (index_t k1 = 0; k1 < m_NE1; ++k1) {
1299                        for (index_t k0 = 0; k0 < m_NE0; ++k0) {
1300                            double* o = out.getSampleDataRW(m_faceOffset[5]+INDEX2(k0,k1,m_NE0));
1301                            fill(o, o+numQuad, size);
1302                        }
1303                    }
1304                }
1305            } // end of parallel section
1306    
1307        } else {
1308            stringstream msg;
1309            msg << "setToSize() not implemented for "
1310                << functionSpaceTypeAsString(out.getFunctionSpace().getTypeCode());
1311            throw RipleyException(msg.str());
1312      }      }
1313  }  }
1314    
# Line 384  Paso_SystemMatrixPattern* Brick::getPatt Line 1318  Paso_SystemMatrixPattern* Brick::getPatt
1318      if (reducedRowOrder || reducedColOrder)      if (reducedRowOrder || reducedColOrder)
1319          throw RipleyException("getPattern() not implemented for reduced order");          throw RipleyException("getPattern() not implemented for reduced order");
1320    
1321      throw RipleyException("getPattern() not implemented");      return m_pattern;
1322  }  }
1323    
1324  void Brick::Print_Mesh_Info(const bool full) const  void Brick::Print_Mesh_Info(const bool full) const
# Line 460  pair<double,double> Brick::getFirstCoord Line 1394  pair<double,double> Brick::getFirstCoord
1394      throw RipleyException("getFirstCoordAndSpacing(): invalid argument");      throw RipleyException("getFirstCoordAndSpacing(): invalid argument");
1395  }  }
1396    
1397    //protected
1398    dim_t Brick::getNumDOF() const
1399    {
1400        return (m_gNE0+1)/m_NX*(m_gNE1+1)/m_NY*(m_gNE2+1)/m_NZ;
1401    }
1402    
1403  //protected  //protected
1404  dim_t Brick::getNumFaceElements() const  dim_t Brick::getNumFaceElements() const
1405  {  {
1406        const IndexVector faces = getNumFacesPerBoundary();
1407      dim_t n=0;      dim_t n=0;
1408      //left      for (size_t i=0; i<faces.size(); i++)
1409      if (m_offset0==0)          n+=faces[i];
         n+=m_NE1*m_NE2;  
     //right  
     if (m_mpiInfo->rank%m_NX==m_NX-1)  
         n+=m_NE1*m_NE2;  
     //bottom  
     if (m_offset1==0)  
         n+=m_NE0*m_NE2;  
     //top  
     if (m_mpiInfo->rank%(m_NX*m_NY)/m_NX==m_NY-1)  
         n+=m_NE0*m_NE2;  
     //front  
     if (m_offset2==0)  
         n+=m_NE0*m_NE1;  
     //back  
     if (m_mpiInfo->rank/(m_NX*m_NY)==m_NZ-1)  
         n+=m_NE0*m_NE1;  
   
1410      return n;      return n;
1411  }  }
1412    
# Line 514  void Brick::assembleCoordinates(escript: Line 1437  void Brick::assembleCoordinates(escript:
1437      }      }
1438  }  }
1439    
1440    //protected
1441    dim_t Brick::insertNeighbourNodes(IndexVector& index, index_t node) const
1442    {
1443        const dim_t nDOF0 = (m_gNE0+1)/m_NX;
1444        const dim_t nDOF1 = (m_gNE1+1)/m_NY;
1445        const dim_t nDOF2 = (m_gNE2+1)/m_NZ;
1446        const int x=node%nDOF0;
1447        const int y=node%(nDOF0*nDOF1)/nDOF0;
1448        const int z=node/(nDOF0*nDOF1);
1449        int num=0;
1450        // loop through potential neighbours and add to index if positions are
1451        // within bounds
1452        for (int i2=-1; i2<2; i2++) {
1453            for (int i1=-1; i1<2; i1++) {
1454                for (int i0=-1; i0<2; i0++) {
1455                    // skip node itself
1456                    if (i0==0 && i1==0 && i2==0)
1457                        continue;
1458                    // location of neighbour node
1459                    const int nx=x+i0;
1460                    const int ny=y+i1;
1461                    const int nz=z+i2;
1462                    if (nx>=0 && ny>=0 && nz>=0
1463                            && nx<nDOF0 && ny<nDOF1 && nz<nDOF2) {
1464                        index.push_back(nz*nDOF0*nDOF1+ny*nDOF0+nx);
1465                        num++;
1466                    }
1467                }
1468            }
1469        }
1470    
1471        return num;
1472    }
1473    
1474    //protected
1475    void Brick::nodesToDOF(escript::Data& out, escript::Data& in) const
1476    {
1477        const dim_t numComp = in.getDataPointSize();
1478        out.requireWrite();
1479    
1480        const index_t left = (m_offset0==0 ? 0 : 1);
1481        const index_t bottom = (m_offset1==0 ? 0 : 1);
1482        const index_t front = (m_offset2==0 ? 0 : 1);
1483        const dim_t nDOF0 = (m_gNE0+1)/m_NX;
1484        const dim_t nDOF1 = (m_gNE1+1)/m_NY;
1485        const dim_t nDOF2 = (m_gNE2+1)/m_NZ;
1486    #pragma omp parallel for
1487        for (index_t i=0; i<nDOF2; i++) {
1488            for (index_t j=0; j<nDOF1; j++) {
1489                for (index_t k=0; k<nDOF0; k++) {
1490                    const index_t n=k+left+(j+bottom)*m_N0+(i+front)*m_N0*m_N1;
1491                    const double* src=in.getSampleDataRO(n);
1492                    copy(src, src+numComp, out.getSampleDataRW(k+j*nDOF0+i*nDOF0*nDOF1));
1493                }
1494            }
1495        }
1496    }
1497    
1498    //protected
1499    void Brick::dofToNodes(escript::Data& out, escript::Data& in) const
1500    {
1501        const dim_t numComp = in.getDataPointSize();
1502        Paso_Coupler* coupler = Paso_Coupler_alloc(m_connector, numComp);
1503        in.requireWrite();
1504        Paso_Coupler_startCollect(coupler, in.getSampleDataRW(0));
1505    
1506        const dim_t numDOF = getNumDOF();
1507        out.requireWrite();
1508        const double* buffer = Paso_Coupler_finishCollect(coupler);
1509    
1510    #pragma omp parallel for
1511        for (index_t i=0; i<getNumNodes(); i++) {
1512            const double* src=(m_dofMap[i]<numDOF ?
1513                    in.getSampleDataRO(m_dofMap[i])
1514                    : &buffer[(m_dofMap[i]-numDOF)*numComp]);
1515            copy(src, src+numComp, out.getSampleDataRW(i));
1516        }
1517    }
1518    
1519  //private  //private
1520  void Brick::populateSampleIds()  void Brick::populateSampleIds()
1521  {  {
1522      // identifiers are ordered from left to right, bottom to top, front to back      // identifiers are ordered from left to right, bottom to top, front to back
1523      // on each rank, except for the shared nodes which are owned by the rank      // globally
     // below / to the left / to the front of the current rank  
1524    
1525      // build node distribution vector first.      // build node distribution vector first.
     // m_nodeDistribution[i] is the first node id on rank i, that is  
1526      // rank i owns m_nodeDistribution[i+1]-nodeDistribution[i] nodes      // rank i owns m_nodeDistribution[i+1]-nodeDistribution[i] nodes
1527      m_nodeDistribution.assign(m_mpiInfo->size+1, 0);      m_nodeDistribution.assign(m_mpiInfo->size+1, 0);
1528      m_nodeDistribution[1]=getNumNodes();      const dim_t numDOF=getNumDOF();
1529      for (dim_t k=1; k<m_mpiInfo->size-1; k++) {      for (dim_t k=1; k<m_mpiInfo->size; k++) {
1530          const index_t x = k%m_NX;          m_nodeDistribution[k]=k*numDOF;
         const index_t y = k%(m_NX*m_NY)/m_NX;  
         const index_t z = k/(m_NX*m_NY);  
         index_t numNodes=getNumNodes();  
         if (x>0)  
             numNodes-=m_N1*m_N2;  
         if (y>0)  
             numNodes-=m_N0*m_N2;  
         if (z>0)  
             numNodes-=m_N0*m_N1;  
         // if an edge was subtracted twice add it back  
         if (x>0 && y>0)  
             numNodes+=m_N2;  
         if (x>0 && z>0)  
             numNodes+=m_N1;  
         if (y>0 && z>0)  
             numNodes+=m_N0;  
         // the corner node was removed 3x and added back 3x, so subtract it  
         if (x>0 && y>0 && z>0)  
             numNodes--;  
         m_nodeDistribution[k+1]=m_nodeDistribution[k]+numNodes;  
1531      }      }
1532      m_nodeDistribution[m_mpiInfo->size]=getNumDataPointsGlobal();      m_nodeDistribution[m_mpiInfo->size]=getNumDataPointsGlobal();
   
1533      m_nodeId.resize(getNumNodes());      m_nodeId.resize(getNumNodes());
1534        m_dofId.resize(numDOF);
1535        m_elementId.resize(getNumElements());
1536        m_faceId.resize(getNumFaceElements());
1537    
1538      // the bottom, left and front planes are not owned by this rank so the  #pragma omp parallel
1539      // identifiers need to be computed accordingly      {
1540    #pragma omp for nowait
1541            // nodes
1542            for (dim_t i2=0; i2<m_N2; i2++) {
1543                for (dim_t i1=0; i1<m_N1; i1++) {
1544                    for (dim_t i0=0; i0<m_N0; i0++) {
1545                        m_nodeId[i0+i1*m_N0+i2*m_N0*m_N1] =
1546                            (m_offset2+i2)*(m_gNE0+1)*(m_gNE1+1)
1547                            +(m_offset1+i1)*(m_gNE0+1)
1548                            +m_offset0+i0;
1549                    }
1550                }
1551            }
1552    
1553            // degrees of freedom
1554    #pragma omp for nowait
1555            for (dim_t k=0; k<numDOF; k++)
1556                m_dofId[k] = m_nodeDistribution[m_mpiInfo->rank]+k;
1557    
1558            // elements
1559    #pragma omp for nowait
1560            for (dim_t i2=0; i2<m_NE2; i2++) {
1561                for (dim_t i1=0; i1<m_NE1; i1++) {
1562                    for (dim_t i0=0; i0<m_NE0; i0++) {
1563                        m_elementId[i0+i1*m_NE0+i2*m_NE0*m_NE1] =
1564                            (m_offset2+i2)*m_gNE0*m_gNE1
1565                            +(m_offset1+i1)*m_gNE0
1566                            +m_offset0+i0;
1567                    }
1568                }
1569            }
1570    
1571            // face elements
1572    #pragma omp for
1573            for (dim_t k=0; k<getNumFaceElements(); k++)
1574                m_faceId[k]=k;
1575        } // end parallel section
1576    
1577        m_nodeTags.assign(getNumNodes(), 0);
1578        updateTagsInUse(Nodes);
1579    
1580        m_elementTags.assign(getNumElements(), 0);
1581        updateTagsInUse(Elements);
1582    
1583        // generate face offset vector and set face tags
1584        const IndexVector facesPerEdge = getNumFacesPerBoundary();
1585        const index_t LEFT=1, RIGHT=2, BOTTOM=10, TOP=20, FRONT=100, BACK=200;
1586        const index_t faceTag[] = { LEFT, RIGHT, BOTTOM, TOP, FRONT, BACK };
1587        m_faceOffset.assign(facesPerEdge.size(), -1);
1588        m_faceTags.clear();
1589        index_t offset=0;
1590        for (size_t i=0; i<facesPerEdge.size(); i++) {
1591            if (facesPerEdge[i]>0) {
1592                m_faceOffset[i]=offset;
1593                offset+=facesPerEdge[i];
1594                m_faceTags.insert(m_faceTags.end(), facesPerEdge[i], faceTag[i]);
1595            }
1596        }
1597        setTagMap("left", LEFT);
1598        setTagMap("right", RIGHT);
1599        setTagMap("bottom", BOTTOM);
1600        setTagMap("top", TOP);
1601        setTagMap("front", FRONT);
1602        setTagMap("back", BACK);
1603        updateTagsInUse(FaceElements);
1604    }
1605    
1606    //private
1607    void Brick::createPattern()
1608    {
1609        const dim_t nDOF0 = (m_gNE0+1)/m_NX;
1610        const dim_t nDOF1 = (m_gNE1+1)/m_NY;
1611        const dim_t nDOF2 = (m_gNE2+1)/m_NZ;
1612      const index_t left = (m_offset0==0 ? 0 : 1);      const index_t left = (m_offset0==0 ? 0 : 1);
1613      const index_t bottom = (m_offset1==0 ? 0 : 1);      const index_t bottom = (m_offset1==0 ? 0 : 1);
1614      const index_t front = (m_offset2==0 ? 0 : 1);      const index_t front = (m_offset2==0 ? 0 : 1);
1615    
1616      // case 1: all nodes on left plane are owned by rank on the left      // populate node->DOF mapping with own degrees of freedom.
1617      if (left>0) {      // The rest is assigned in the loop further down
1618          const int neighbour=m_mpiInfo->rank-1;      m_dofMap.assign(getNumNodes(), 0);
         const index_t leftN0=(neighbour%m_NX == 0 ? m_N0 : m_N0-1);  
         const index_t leftN1=(neighbour%(m_NX*m_NY)/m_NX==0 ? m_N1 : m_N1-1);  
1619  #pragma omp parallel for  #pragma omp parallel for
1620          for (dim_t i2=front; i2<m_N2; i2++) {      for (index_t i=front; i<m_N2; i++) {
1621              for (dim_t i1=bottom; i1<m_N1; i1++) {          for (index_t j=bottom; j<m_N1; j++) {
1622                  m_nodeId[i1*m_N0+i2*m_N0*m_N1]=m_nodeDistribution[neighbour]              for (index_t k=left; k<m_N0; k++) {
1623                      + (i1-bottom+1)*leftN0                  m_dofMap[i*m_N0*m_N1+j*m_N0+k]=(i-front)*nDOF0*nDOF1+(j-bottom)*nDOF0+k-left;
                     + (i2-front)*leftN0*leftN1 - 1;  
1624              }              }
1625          }          }
1626      }      }
1627      // case 2: all nodes on bottom plane are owned by rank below  
1628      if (bottom>0) {      // build list of shared components and neighbours by looping through
1629          const int neighbour=m_mpiInfo->rank-m_NX;      // all potential neighbouring ranks and checking if positions are
1630          const index_t bottomN0=(neighbour%m_NX == 0 ? m_N0 : m_N0-1);      // within bounds
1631          const index_t bottomN1=(neighbour%(m_NX*m_NY)/m_NX==0 ? m_N1 : m_N1-1);      const dim_t numDOF=nDOF0*nDOF1*nDOF2;
1632  #pragma omp parallel for      vector<IndexVector> colIndices(numDOF); // for the couple blocks
1633          for (dim_t i2=front; i2<m_N2; i2++) {      RankVector neighbour;
1634              for (dim_t i0=left; i0<m_N0; i0++) {      IndexVector offsetInShared(1,0);
1635                  m_nodeId[i0+i2*m_N0*m_N1]=m_nodeDistribution[neighbour]      IndexVector sendShared, recvShared;
1636                      + bottomN0*(bottomN1-1)      int numShared=0;
1637                      + (i2-front)*bottomN0*bottomN1 + i0-left;      const int x=m_mpiInfo->rank%m_NX;
1638        const int y=m_mpiInfo->rank%(m_NX*m_NY)/m_NX;
1639        const int z=m_mpiInfo->rank/(m_NX*m_NY);
1640        for (int i2=-1; i2<2; i2++) {
1641            for (int i1=-1; i1<2; i1++) {
1642                for (int i0=-1; i0<2; i0++) {
1643                    // skip this rank
1644                    if (i0==0 && i1==0 && i2==0)
1645                        continue;
1646                    // location of neighbour rank
1647                    const int nx=x+i0;
1648                    const int ny=y+i1;
1649                    const int nz=z+i2;
1650                    if (nx>=0 && ny>=0 && nz>=0 && nx<m_NX && ny<m_NY && nz<m_NZ) {
1651                        neighbour.push_back(nz*m_NX*m_NY+ny*m_NX+nx);
1652                        if (i0==0 && i1==0) {
1653                            // sharing front or back plane
1654                            offsetInShared.push_back(offsetInShared.back()+nDOF0*nDOF1);
1655                            for (dim_t i=0; i<nDOF1; i++) {
1656                                const int firstDOF=(i2==-1 ? i*nDOF0
1657                                        : i*nDOF0 + nDOF0*nDOF1*(nDOF2-1));
1658                                const int firstNode=(i2==-1 ? left+(i+bottom)*m_N0
1659                                        : left+(i+bottom)*m_N0+m_N0*m_N1*(m_N2-1));
1660                                for (dim_t j=0; j<nDOF0; j++, numShared++) {
1661                                    sendShared.push_back(firstDOF+j);
1662                                    recvShared.push_back(numDOF+numShared);
1663                                    if (j>0) {
1664                                        if (i>0)
1665                                            colIndices[firstDOF+j-1-nDOF0].push_back(numShared);
1666                                        colIndices[firstDOF+j-1].push_back(numShared);
1667                                        if (i<nDOF1-1)
1668                                            colIndices[firstDOF+j-1+nDOF0].push_back(numShared);
1669                                    }
1670                                    if (i>0)
1671                                        colIndices[firstDOF+j-nDOF0].push_back(numShared);
1672                                    colIndices[firstDOF+j].push_back(numShared);
1673                                    if (i<nDOF1-1)
1674                                        colIndices[firstDOF+j+nDOF0].push_back(numShared);
1675                                    if (j<nDOF0-1) {
1676                                        if (i>0)
1677                                            colIndices[firstDOF+j+1-nDOF0].push_back(numShared);
1678                                        colIndices[firstDOF+j+1].push_back(numShared);
1679                                        if (i<nDOF1-1)
1680                                            colIndices[firstDOF+j+1+nDOF0].push_back(numShared);
1681                                    }
1682                                    m_dofMap[firstNode+j]=numDOF+numShared;
1683                                }
1684                            }
1685                        } else if (i0==0 && i2==0) {
1686                            // sharing top or bottom plane
1687                            offsetInShared.push_back(offsetInShared.back()+nDOF0*nDOF2);
1688                            for (dim_t i=0; i<nDOF2; i++) {
1689                                const int firstDOF=(i1==-1 ? i*nDOF0*nDOF1
1690                                        : nDOF0*((i+1)*nDOF1-1));
1691                                const int firstNode=(i1==-1 ?
1692                                        left+(i+front)*m_N0*m_N1
1693                                        : left+m_N0*((i+1+front)*m_N1-1));
1694                                for (dim_t j=0; j<nDOF0; j++, numShared++) {
1695                                    sendShared.push_back(firstDOF+j);
1696                                    recvShared.push_back(numDOF+numShared);
1697                                    if (j>0) {
1698                                        if (i>0)
1699                                            colIndices[firstDOF+j-1-nDOF0*nDOF1].push_back(numShared);
1700                                        colIndices[firstDOF+j-1].push_back(numShared);
1701                                        if (i<nDOF2-1)
1702                                            colIndices[firstDOF+j-1+nDOF0*nDOF1].push_back(numShared);
1703                                    }
1704                                    if (i>0)
1705                                        colIndices[firstDOF+j-nDOF0*nDOF1].push_back(numShared);
1706                                    colIndices[firstDOF+j].push_back(numShared);
1707                                    if (i<nDOF2-1)
1708                                        colIndices[firstDOF+j+nDOF0*nDOF1].push_back(numShared);
1709                                    if (j<nDOF0-1) {
1710                                        if (i>0)
1711                                            colIndices[firstDOF+j+1-nDOF0*nDOF1].push_back(numShared);
1712                                        colIndices[firstDOF+j+1].push_back(numShared);
1713                                        if (i<nDOF2-1)
1714                                            colIndices[firstDOF+j+1+nDOF0*nDOF1].push_back(numShared);
1715                                    }
1716                                    m_dofMap[firstNode+j]=numDOF+numShared;
1717                                }
1718                            }
1719                        } else if (i1==0 && i2==0) {
1720                            // sharing left or right plane
1721                            offsetInShared.push_back(offsetInShared.back()+nDOF1*nDOF2);
1722                            for (dim_t i=0; i<nDOF2; i++) {
1723                                const int firstDOF=(i0==-1 ? i*nDOF0*nDOF1
1724                                        : nDOF0*(1+i*nDOF1)-1);
1725                                const int firstNode=(i0==-1 ?
1726                                        (bottom+(i+front)*m_N1)*m_N0
1727                                        : (bottom+1+(i+front)*m_N1)*m_N0-1);
1728                                for (dim_t j=0; j<nDOF1; j++, numShared++) {
1729                                    sendShared.push_back(firstDOF+j*nDOF0);
1730                                    recvShared.push_back(numDOF+numShared);
1731                                    if (j>0) {
1732                                        if (i>0)
1733                                            colIndices[firstDOF+(j-1)*nDOF0-nDOF0*nDOF1].push_back(numShared);
1734                                        colIndices[firstDOF+(j-1)*nDOF0].push_back(numShared);
1735                                        if (i<nDOF2-1)
1736                                            colIndices[firstDOF+(j-1)*nDOF0+nDOF0*nDOF1].push_back(numShared);
1737                                    }
1738                                    if (i>0)
1739                                        colIndices[firstDOF+j*nDOF0-nDOF0*nDOF1].push_back(numShared);
1740                                    colIndices[firstDOF+j*nDOF0].push_back(numShared);
1741                                    if (i<nDOF2-1)
1742                                        colIndices[firstDOF+j*nDOF0+nDOF0*nDOF1].push_back(numShared);
1743                                    if (j<nDOF1-1) {
1744                                        if (i>0)
1745                                            colIndices[firstDOF+(j+1)*nDOF0-nDOF0*nDOF1].push_back(numShared);
1746                                        colIndices[firstDOF+(j+1)*nDOF0].push_back(numShared);
1747                                        if (i<nDOF2-1)
1748                                            colIndices[firstDOF+(j+1)*nDOF0+nDOF0*nDOF1].push_back(numShared);
1749                                    }
1750                                    m_dofMap[firstNode+j*m_N0]=numDOF+numShared;
1751                                }
1752                            }
1753                        } else if (i0==0) {
1754                            // sharing an edge in x direction
1755                            offsetInShared.push_back(offsetInShared.back()+nDOF0);
1756                            const int firstDOF=(i1+1)/2*nDOF0*(nDOF1-1)
1757                                               +(i2+1)/2*nDOF0*nDOF1*(nDOF2-1);
1758                            const int firstNode=(i1+1)/2*m_N0*(m_N1-1)
1759                                                +(i2+1)/2*m_N0*m_N1*(m_N2-1);
1760                            for (dim_t i=0; i<nDOF0; i++, numShared++) {
1761                                sendShared.push_back(firstDOF+i);
1762                                recvShared.push_back(numDOF+numShared);
1763                                if (i>0)
1764                                    colIndices[firstDOF+i-1].push_back(numShared);
1765                                colIndices[firstDOF+i].push_back(numShared);
1766                                if (i<nDOF0-1)
1767                                    colIndices[firstDOF+i+1].push_back(numShared);
1768                                m_dofMap[firstNode+i]=numDOF+numShared;
1769                            }
1770                        } else if (i1==0) {
1771                            // sharing an edge in y direction
1772                            offsetInShared.push_back(offsetInShared.back()+nDOF1);
1773                            const int firstDOF=(i0+1)/2*(nDOF0-1)
1774                                               +(i2+1)/2*nDOF0*nDOF1*(nDOF2-1);
1775                            const int firstNode=(i0+1)/2*(m_N0-1)
1776                                                +(i2+1)/2*m_N0*m_N1*(m_N2-1);
1777                            for (dim_t i=0; i<nDOF1; i++, numShared++) {
1778                                sendShared.push_back(firstDOF+i*nDOF0);
1779                                recvShared.push_back(numDOF+numShared);
1780                                if (i>0)
1781                                    colIndices[firstDOF+(i-1)*nDOF0].push_back(numShared);
1782                                colIndices[firstDOF+i*nDOF0].push_back(numShared);
1783                                if (i<nDOF1-1)
1784                                    colIndices[firstDOF+(i+1)*nDOF0].push_back(numShared);
1785                                m_dofMap[firstNode+i*m_N0]=numDOF+numShared;
1786                            }
1787                        } else if (i2==0) {
1788                            // sharing an edge in z direction
1789                            offsetInShared.push_back(offsetInShared.back()+nDOF2);
1790                            const int firstDOF=(i0+1)/2*(nDOF0-1)
1791                                               +(i1+1)/2*nDOF0*(nDOF1-1);
1792                            const int firstNode=(i0+1)/2*(m_N0-1)
1793                                                +(i1+1)/2*m_N0*(m_N1-1);
1794                            for (dim_t i=0; i<nDOF2; i++, numShared++) {
1795                                sendShared.push_back(firstDOF+i*nDOF0*nDOF1);
1796                                recvShared.push_back(numDOF+numShared);
1797                                if (i>0)
1798                                    colIndices[firstDOF+(i-1)*nDOF0*nDOF1].push_back(numShared);
1799                                colIndices[firstDOF+i*nDOF0*nDOF1].push_back(numShared);
1800                                if (i<nDOF2-1)
1801                                    colIndices[firstDOF+(i+1)*nDOF0*nDOF1].push_back(numShared);
1802                                m_dofMap[firstNode+i*m_N0*m_N1]=numDOF+numShared;
1803                            }
1804                        } else {
1805                            // sharing a node
1806                            const int dof=(i0+1)/2*(nDOF0-1)
1807                                          +(i1+1)/2*nDOF0*(nDOF1-1)
1808                                          +(i2+1)/2*nDOF0*nDOF1*(nDOF2-1);
1809                            const int node=(i0+1)/2*(m_N0-1)
1810                                           +(i1+1)/2*m_N0*(m_N1-1)
1811                                           +(i2+1)/2*m_N0*m_N1*(m_N2-1);
1812                            offsetInShared.push_back(offsetInShared.back()+1);
1813                            sendShared.push_back(dof);
1814                            recvShared.push_back(numDOF+numShared);
1815                            colIndices[dof].push_back(numShared);
1816                            m_dofMap[node]=numDOF+numShared;
1817                            ++numShared;
1818                        }
1819                    }
1820              }              }
1821          }          }
1822      }      }
1823      // case 3: all nodes on front plane are owned by rank in front  
1824      if (front>0) {      // create connector
1825          const int neighbour=m_mpiInfo->rank-m_NX*m_NY;      Paso_SharedComponents *snd_shcomp = Paso_SharedComponents_alloc(
1826          const index_t N0=(neighbour%m_NX == 0 ? m_N0 : m_N0-1);              numDOF, neighbour.size(), &neighbour[0], &sendShared[0],
1827          const index_t N1=(neighbour%(m_NX*m_NY)/m_NX==0 ? m_N1 : m_N1-1);              &offsetInShared[0], 1, 0, m_mpiInfo);
1828          const index_t N2=(neighbour/(m_NX*m_NY)==0 ? m_N2 : m_N2-1);      Paso_SharedComponents *rcv_shcomp = Paso_SharedComponents_alloc(
1829  #pragma omp parallel for              numDOF, neighbour.size(), &neighbour[0], &recvShared[0],
1830          for (dim_t i1=bottom; i1<m_N1; i1++) {              &offsetInShared[0], 1, 0, m_mpiInfo);
1831              for (dim_t i0=left; i0<m_N0; i0++) {      m_connector = Paso_Connector_alloc(snd_shcomp, rcv_shcomp);
1832                  m_nodeId[i0+i1*m_N0]=m_nodeDistribution[neighbour]      Paso_SharedComponents_free(snd_shcomp);
1833                      + N0*N1*(N2-1)+(i1-bottom)*N0 + i0-left;      Paso_SharedComponents_free(rcv_shcomp);
1834              }  
1835          }      // create main and couple blocks
1836        Paso_Pattern *mainPattern = createMainPattern();
1837        Paso_Pattern *colPattern, *rowPattern;
1838        createCouplePatterns(colIndices, numShared, &colPattern, &rowPattern);
1839    
1840        // allocate paso distribution
1841        Paso_Distribution* distribution = Paso_Distribution_alloc(m_mpiInfo,
1842                const_cast<index_t*>(&m_nodeDistribution[0]), 1, 0);
1843    
1844        // finally create the system matrix
1845        m_pattern = Paso_SystemMatrixPattern_alloc(MATRIX_FORMAT_DEFAULT,
1846                distribution, distribution, mainPattern, colPattern, rowPattern,
1847                m_connector, m_connector);
1848    
1849        Paso_Distribution_free(distribution);
1850    
1851        // useful debug output
1852        /*
1853        cout << "--- rcv_shcomp ---" << endl;
1854        cout << "numDOF=" << numDOF << ", numNeighbors=" << neighbour.size() << endl;
1855        for (size_t i=0; i<neighbour.size(); i++) {
1856            cout << "neighbor[" << i << "]=" << neighbour[i]
1857                << " offsetInShared[" << i+1 << "]=" << offsetInShared[i+1] << endl;
1858      }      }
1859      // case 4: nodes on front bottom edge are owned by the corresponding rank      for (size_t i=0; i<recvShared.size(); i++) {
1860      if (front>0 && bottom>0) {          cout << "shared[" << i << "]=" << recvShared[i] << endl;
         const int neighbour=m_mpiInfo->rank-m_NX*(m_NY+1);  
         const index_t N0=(neighbour%m_NX == 0 ? m_N0 : m_N0-1);  
         const index_t N1=(neighbour%(m_NX*m_NY)/m_NX==0 ? m_N1 : m_N1-1);  
         const index_t N2=(neighbour/(m_NX*m_NY)==0 ? m_N2 : m_N2-1);  
 #pragma omp parallel for  
         for (dim_t i0=left; i0<m_N0; i0++) {  
             m_nodeId[i0]=m_nodeDistribution[neighbour]  
                 + N0*N1*(N2-1)+(N1-1)*N0 + i0-left;  
         }  
1861      }      }
1862      // case 5: nodes on left bottom edge are owned by the corresponding rank      cout << "--- snd_shcomp ---" << endl;
1863      if (left>0 && bottom>0) {      for (size_t i=0; i<sendShared.size(); i++) {
1864          const int neighbour=m_mpiInfo->rank-m_NX-1;          cout << "shared[" << i << "]=" << sendShared[i] << endl;
         const index_t N0=(neighbour%m_NX == 0 ? m_N0 : m_N0-1);  
         const index_t N1=(neighbour%(m_NX*m_NY)/m_NX==0 ? m_N1 : m_N1-1);  
 #pragma omp parallel for  
         for (dim_t i2=front; i2<m_N2; i2++) {  
             m_nodeId[i2*m_N0*m_N1]=m_nodeDistribution[neighbour]  
                 + (1+i2-front)*N0*N1-1;  
         }  
1865      }      }
1866      // case 6: nodes on left front edge are owned by the corresponding rank      cout << "--- dofMap ---" << endl;
1867      if (left>0 && front>0) {      for (size_t i=0; i<m_dofMap.size(); i++) {
1868          const int neighbour=m_mpiInfo->rank-m_NX*m_NY-1;          cout << "m_dofMap[" << i << "]=" << m_dofMap[i] << endl;
1869          const index_t N0=(neighbour%m_NX == 0 ? m_N0 : m_N0-1);      }
1870          const index_t N1=(neighbour%(m_NX*m_NY)/m_NX==0 ? m_N1 : m_N1-1);      cout << "--- colIndices ---" << endl;
1871          const index_t N2=(neighbour/(m_NX*m_NY)==0 ? m_N2 : m_N2-1);      for (size_t i=0; i<colIndices.size(); i++) {
1872  #pragma omp parallel for          cout << "colIndices[" << i << "].size()=" << colIndices[i].size() << endl;
         for (dim_t i1=bottom; i1<m_N1; i1++) {  
             m_nodeId[i1*m_N0]=m_nodeDistribution[neighbour]  
                 + N0*N1*(N2-1)+N0-1+(i1-bottom)*N0;  
         }  
     }  
     // case 7: bottom-left-front corner node owned by corresponding rank  
     if (left>0 && bottom>0 && front>0) {  
         const int neighbour=m_mpiInfo->rank-m_NX*(m_NY+1)-1;  
         const index_t N0=(neighbour%m_NX == 0 ? m_N0 : m_N0-1);  
         const index_t N1=(neighbour%(m_NX*m_NY)/m_NX==0 ? m_N1 : m_N1-1);  
         const index_t N2=(neighbour/(m_NX*m_NY) == 0 ? m_N2 : m_N2-1);  
         m_nodeId[0]=m_nodeDistribution[neighbour]+N0*N1*N2-1;  
1873      }      }
1874        */
1875    
1876      // the rest of the id's are contiguous      /*
1877      const index_t firstId=m_nodeDistribution[m_mpiInfo->rank];      cout << "--- main_pattern ---" << endl;
1878  #pragma omp parallel for      cout << "M=" << mainPattern->numOutput << ", N=" << mainPattern->numInput << endl;
1879      for (dim_t i2=front; i2<m_N2; i2++) {      for (size_t i=0; i<mainPattern->numOutput+1; i++) {
1880          for (dim_t i1=bottom; i1<m_N1; i1++) {          cout << "ptr[" << i << "]=" << mainPattern->ptr[i] << endl;
             for (dim_t i0=left; i0<m_N0; i0++) {  
                 m_nodeId[i0+i1*m_N0+i2*m_N0*m_N1] = firstId+i0-left  
                     +(i1-bottom)*(m_N0-left)  
                     +(i2-front)*(m_N0-left)*(m_N1-bottom);  
             }  
         }  
1881      }      }
1882        for (size_t i=0; i<mainPattern->ptr[mainPattern->numOutput]; i++) {
1883            cout << "index[" << i << "]=" << mainPattern->index[i] << endl;
1884        }
1885        */
1886    
1887      // elements      /*
1888      m_elementId.resize(getNumElements());      cout << "--- colCouple_pattern ---" << endl;
1889  #pragma omp parallel for      cout << "M=" << colPattern->numOutput << ", N=" << colPattern->numInput << endl;
1890      for (dim_t k=0; k<getNumElements(); k++) {      for (size_t i=0; i<colPattern->numOutput+1; i++) {
1891          m_elementId[k]=k;          cout << "ptr[" << i << "]=" << colPattern->ptr[i] << endl;
1892        }
1893        for (size_t i=0; i<colPattern->ptr[colPattern->numOutput]; i++) {
1894            cout << "index[" << i << "]=" << colPattern->index[i] << endl;
1895      }      }
1896        */
1897    
1898      // face elements      /*
1899      m_faceId.resize(getNumFaceElements());      cout << "--- rowCouple_pattern ---" << endl;
1900  #pragma omp parallel for      cout << "M=" << rowPattern->numOutput << ", N=" << rowPattern->numInput << endl;
1901      for (dim_t k=0; k<getNumFaceElements(); k++) {      for (size_t i=0; i<rowPattern->numOutput+1; i++) {
1902          m_faceId[k]=k;          cout << "ptr[" << i << "]=" << rowPattern->ptr[i] << endl;
1903      }      }
1904        for (size_t i=0; i<rowPattern->ptr[rowPattern->numOutput]; i++) {
1905            cout << "index[" << i << "]=" << rowPattern->index[i] << endl;
1906        }
1907        */
1908    
1909        Paso_Pattern_free(mainPattern);
1910        Paso_Pattern_free(colPattern);
1911        Paso_Pattern_free(rowPattern);
1912  }  }
1913    
1914  //protected  //protected
1915  void Brick::interpolateNodesOnElements(escript::Data& out, escript::Data& in) const  void Brick::interpolateNodesOnElements(escript::Data& out, escript::Data& in,
1916                                           bool reduced) const
1917  {  {
1918      const dim_t numComp = in.getDataPointSize();      const dim_t numComp = in.getDataPointSize();
1919      /* GENERATOR SNIP_INTERPOLATE_ELEMENTS TOP */      if (reduced) {
1920      const double tmp0_3 = 0.0094373878376559314545;          out.requireWrite();
1921      const double tmp0_2 = 0.035220810900864519624;          /*** GENERATOR SNIP_INTERPOLATE_REDUCED_ELEMENTS TOP */
1922      const double tmp0_1 = 0.13144585576580214704;          const double c0 = .125;
1923      const double tmp0_0 = 0.49056261216234406855;  #pragma omp parallel for
1924            for (index_t k2=0; k2 < m_NE2; ++k2) {
1925                for (index_t k1=0; k1 < m_NE1; ++k1) {
1926                    for (index_t k0=0; k0 < m_NE0; ++k0) {
1927                        const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,k2, m_N0,m_N1));
1928                        const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,k2+1, m_N0,m_N1));
1929                        const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,k2+1, m_N0,m_N1));
1930                        const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,k2+1, m_N0,m_N1));
1931                        const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,k2, m_N0,m_N1));
1932                        const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,k2, m_N0,m_N1));
1933                        const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,k2, m_N0,m_N1));
1934                        const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,k2+1, m_N0,m_N1));
1935                        double* o = out.getSampleDataRW(INDEX3(k0,k1,k2,m_NE0,m_NE1));
1936                        for (index_t i=0; i < numComp; ++i) {
1937                            o[INDEX2(i,numComp,0)] = c0*(f_000[i] + f_001[i] + f_010[i] + f_011[i] + f_100[i] + f_101[i] + f_110[i] + f_111[i]);
1938                        } /* end of component loop i */
1939                    } /* end of k0 loop */
1940                } /* end of k1 loop */
1941            } /* end of k2 loop */
1942            /* GENERATOR SNIP_INTERPOLATE_REDUCED_ELEMENTS BOTTOM */
1943        } else {
1944            out.requireWrite();
1945            /*** GENERATOR SNIP_INTERPOLATE_ELEMENTS TOP */
1946            const double c0 = .0094373878376559314545;
1947            const double c1 = .035220810900864519624;
1948            const double c2 = .13144585576580214704;
1949            const double c3 = .49056261216234406855;
1950  #pragma omp parallel for  #pragma omp parallel for
1951      for (index_t k2=0; k2 < m_NE2; ++k2) {          for (index_t k2=0; k2 < m_NE2; ++k2) {
1952          for (index_t k1=0; k1 < m_NE1; ++k1) {              for (index_t k1=0; k1 < m_NE1; ++k1) {
1953              for (index_t k0=0; k0 < m_NE0; ++k0) {                  for (index_t k0=0; k0 < m_NE0; ++k0) {
1954                  const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,k2, m_N0,m_N1));                      const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,k2, m_N0,m_N1));
1955                  const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,k2+1, m_N0,m_N1));                      const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,k2+1, m_N0,m_N1));
1956                  const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,k2+1, m_N0,m_N1));                      const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,k2+1, m_N0,m_N1));
1957                  const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,k2+1, m_N0,m_N1));                      const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,k2+1, m_N0,m_N1));
1958                  const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,k2, m_N0,m_N1));                      const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,k2, m_N0,m_N1));
1959                  const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,k2, m_N0,m_N1));                      const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,k2, m_N0,m_N1));
1960                  const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,k2, m_N0,m_N1));                      const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,k2, m_N0,m_N1));
1961                  const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,k2+1, m_N0,m_N1));                      const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,k2+1, m_N0,m_N1));
1962                  double* o = out.getSampleDataRW(INDEX3(k0,k1,k2,m_NE0,m_NE1));                      double* o = out.getSampleDataRW(INDEX3(k0,k1,k2,m_NE0,m_NE1));
1963                  for (index_t i=0; i < numComp; ++i) {                      for (index_t i=0; i < numComp; ++i) {
1964                      o[INDEX2(i,numComp,0)] = f_000[i]*tmp0_0 + f_111[i]*tmp0_3 + tmp0_1*(f_001[i] + f_010[i] + f_100[i]) + tmp0_2*(f_011[i] + f_101[i] + f_110[i]);                          o[INDEX2(i,numComp,0)] = f_000[i]*c3 + f_111[i]*c0 + c2*(f_001[i] + f_010[i] + f_100[i]) + c1*(f_011[i] + f_101[i] + f_110[i]);
1965                      o[INDEX2(i,numComp,1)] = f_011[i]*tmp0_3 + f_100[i]*tmp0_0 + tmp0_1*(f_000[i] + f_101[i] + f_110[i]) + tmp0_2*(f_001[i] + f_010[i] + f_111[i]);                          o[INDEX2(i,numComp,1)] = f_011[i]*c0 + f_100[i]*c3 + c2*(f_000[i] + f_101[i] + f_110[i]) + c1*(f_001[i] + f_010[i] + f_111[i]);
1966                      o[INDEX2(i,numComp,2)] = f_010[i]*tmp0_0 + f_101[i]*tmp0_3 + tmp0_1*(f_000[i] + f_011[i] + f_110[i]) + tmp0_2*(f_001[i] + f_100[i] + f_111[i]);                          o[INDEX2(i,numComp,2)] = f_010[i]*c3 + f_101[i]*c0 + c2*(f_000[i] + f_011[i] + f_110[i]) + c1*(f_001[i] + f_100[i] + f_111[i]);
1967                      o[INDEX2(i,numComp,3)] = f_001[i]*tmp0_3 + f_110[i]*tmp0_0 + tmp0_1*(f_010[i] + f_100[i] + f_111[i]) + tmp0_2*(f_000[i] + f_011[i] + f_101[i]);                          o[INDEX2(i,numComp,3)] = f_001[i]*c0 + f_110[i]*c3 + c2*(f_010[i] + f_100[i] + f_111[i]) + c1*(f_000[i] + f_011[i] + f_101[i]);
1968                      o[INDEX2(i,numComp,4)] = f_001[i]*tmp0_0 + f_110[i]*tmp0_3 + tmp0_1*(f_000[i] + f_011[i] + f_101[i]) + tmp0_2*(f_010[i] + f_100[i] + f_111[i]);                          o[INDEX2(i,numComp,4)] = f_001[i]*c3 + f_110[i]*c0 + c2*(f_000[i] + f_011[i] + f_101[i]) + c1*(f_010[i] + f_100[i] + f_111[i]);
1969                      o[INDEX2(i,numComp,5)] = f_010[i]*tmp0_3 + f_101[i]*tmp0_0 + tmp0_1*(f_001[i] + f_100[i] + f_111[i]) + tmp0_2*(f_000[i] + f_011[i] + f_110[i]);                          o[INDEX2(i,numComp,5)] = f_010[i]*c0 + f_101[i]*c3 + c2*(f_001[i] + f_100[i] + f_111[i]) + c1*(f_000[i] + f_011[i] + f_110[i]);
1970                      o[INDEX2(i,numComp,6)] = f_011[i]*tmp0_0 + f_100[i]*tmp0_3 + tmp0_1*(f_001[i] + f_010[i] + f_111[i]) + tmp0_2*(f_000[i] + f_101[i] + f_110[i]);                          o[INDEX2(i,numComp,6)] = f_011[i]*c3 + f_100[i]*c0 + c2*(f_001[i] + f_010[i] + f_111[i]) + c1*(f_000[i] + f_101[i] + f_110[i]);
1971                      o[INDEX2(i,numComp,7)] = f_000[i]*tmp0_3 + f_111[i]*tmp0_0 + tmp0_1*(f_011[i] + f_101[i] + f_110[i]) + tmp0_2*(f_001[i] + f_010[i] + f_100[i]);                          o[INDEX2(i,numComp,7)] = f_000[i]*c0 + f_111[i]*c3 + c2*(f_011[i] + f_101[i] + f_110[i]) + c1*(f_001[i] + f_010[i] + f_100[i]);
1972                  } /* end of component loop i */                      } /* end of component loop i */
1973              } /* end of k0 loop */                  } /* end of k0 loop */
1974          } /* end of k1 loop */              } /* end of k1 loop */
1975      } /* end of k2 loop */          } /* end of k2 loop */
1976      /* GENERATOR SNIP_INTERPOLATE_ELEMENTS BOTTOM */          /* GENERATOR SNIP_INTERPOLATE_ELEMENTS BOTTOM */
1977        }
1978    }
1979    
1980    //protected
1981    void Brick::interpolateNodesOnFaces(escript::Data& out, escript::Data& in,
1982                                        bool reduced) const
1983    {
1984        const dim_t numComp = in.getDataPointSize();
1985        if (reduced) {
1986            out.requireWrite();
1987            const double c0 = .25;
1988    #pragma omp parallel
1989            {
1990                /*** GENERATOR SNIP_INTERPOLATE_REDUCED_FACES TOP */
1991                if (m_faceOffset[0] > -1) {
1992    #pragma omp for nowait
1993                    for (index_t k2=0; k2 < m_NE2; ++k2) {
1994                        for (index_t k1=0; k1 < m_NE1; ++k1) {
1995                            const register double* f_011 = in.getSampleDataRO(INDEX3(0,k1+1,k2+1, m_N0,m_N1));
1996                            const register double* f_010 = in.getSampleDataRO(INDEX3(0,k1+1,k2, m_N0,m_N1));
1997                            const register double* f_001 = in.getSampleDataRO(INDEX3(0,k1,k2+1, m_N0,m_N1));
1998                            const register double* f_000 = in.getSampleDataRO(INDEX3(0,k1,k2, m_N0,m_N1));
1999                            double* o = out.getSampleDataRW(m_faceOffset[0]+INDEX2(k1,k2,m_NE1));
2000                            for (index_t i=0; i < numComp; ++i) {
2001                                o[INDEX2(i,numComp,0)] = c0*(f_000[i] + f_001[i] + f_010[i] + f_011[i]);
2002                            } /* end of component loop i */
2003                        } /* end of k1 loop */
2004                    } /* end of k2 loop */
2005                } /* end of face 0 */
2006                if (m_faceOffset[1] > -1) {
2007    #pragma omp for nowait
2008                    for (index_t k2=0; k2 < m_NE2; ++k2) {
2009                        for (index_t k1=0; k1 < m_NE1; ++k1) {
2010                            const register double* f_110 = in.getSampleDataRO(INDEX3(m_N0-1,k1+1,k2, m_N0,m_N1));
2011                            const register double* f_100 = in.getSampleDataRO(INDEX3(m_N0-1,k1,k2, m_N0,m_N1));
2012                            const register double* f_101 = in.getSampleDataRO(INDEX3(m_N0-1,k1,k2+1, m_N0,m_N1));
2013                            const register double* f_111 = in.getSampleDataRO(INDEX3(m_N0-1,k1+1,k2+1, m_N0,m_N1));
2014                            double* o = out.getSampleDataRW(m_faceOffset[1]+INDEX2(k1,k2,m_NE1));
2015                            for (index_t i=0; i < numComp; ++i) {
2016                                o[INDEX2(i,numComp,0)] = c0*(f_100[i] + f_101[i] + f_110[i] + f_111[i]);
2017                            } /* end of component loop i */
2018                        } /* end of k1 loop */
2019                    } /* end of k2 loop */
2020                } /* end of face 1 */
2021                if (m_faceOffset[2] > -1) {
2022    #pragma omp for nowait
2023                    for (index_t k2=0; k2 < m_NE2; ++k2) {
2024                        for (index_t k0=0; k0 < m_NE0; ++k0) {
2025                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,0,k2, m_N0,m_N1));
2026                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,0,k2+1, m_N0,m_N1));
2027                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,0,k2+1, m_N0,m_N1));
2028                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,0,k2, m_N0,m_N1));
2029                            double* o = out.getSampleDataRW(m_faceOffset[2]+INDEX2(k0,k2,m_NE0));
2030                            for (index_t i=0; i < numComp; ++i) {
2031                                o[INDEX2(i,numComp,0)] = c0*(f_000[i] + f_001[i] + f_100[i] + f_101[i]);
2032                            } /* end of component loop i */
2033                        } /* end of k0 loop */
2034                    } /* end of k2 loop */
2035                } /* end of face 2 */
2036                if (m_faceOffset[3] > -1) {
2037    #pragma omp for nowait
2038                    for (index_t k2=0; k2 < m_NE2; ++k2) {
2039                        for (index_t k0=0; k0 < m_NE0; ++k0) {
2040                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,m_N1-1,k2, m_N0,m_N1));
2041                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,m_N1-1,k2+1, m_N0,m_N1));
2042                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,m_N1-1,k2, m_N0,m_N1));
2043                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,m_N1-1,k2+1, m_N0,m_N1));
2044                            double* o = out.getSampleDataRW(m_faceOffset[3]+INDEX2(k0,k2,m_NE0));
2045                            for (index_t i=0; i < numComp; ++i) {
2046                                o[INDEX2(i,numComp,0)] = c0*(f_010[i] + f_011[i] + f_110[i] + f_111[i]);
2047                            } /* end of component loop i */
2048                        } /* end of k0 loop */
2049                    } /* end of k2 loop */
2050                } /* end of face 3 */
2051                if (m_faceOffset[4] > -1) {
2052    #pragma omp for nowait
2053                    for (index_t k1=0; k1 < m_NE1; ++k1) {
2054                        for (index_t k0=0; k0 < m_NE0; ++k0) {
2055                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,0, m_N0,m_N1));
2056                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,0, m_N0,m_N1));
2057                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,0, m_N0,m_N1));
2058                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,0, m_N0,m_N1));
2059                            double* o = out.getSampleDataRW(m_faceOffset[4]+INDEX2(k0,k1,m_NE0));
2060                            for (index_t i=0; i < numComp; ++i) {
2061                                o[INDEX2(i,numComp,0)] = c0*(f_000[i] + f_010[i] + f_100[i] + f_110[i]);
2062                            } /* end of component loop i */
2063                        } /* end of k0 loop */
2064                    } /* end of k1 loop */
2065                } /* end of face 4 */
2066                if (m_faceOffset[5] > -1) {
2067    #pragma omp for nowait
2068                    for (index_t k1=0; k1 < m_NE1; ++k1) {
2069                        for (index_t k0=0; k0 < m_NE0; ++k0) {
2070                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,m_N2-1, m_N0,m_N1));
2071                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,m_N2-1, m_N0,m_N1));
2072                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,m_N2-1, m_N0,m_N1));
2073                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,m_N2-1, m_N0,m_N1));
2074                            double* o = out.getSampleDataRW(m_faceOffset[5]+INDEX2(k0,k1,m_NE0));
2075                            for (index_t i=0; i < numComp; ++i) {
2076                                o[INDEX2(i,numComp,0)] = c0*(f_001[i] + f_011[i] + f_101[i] + f_111[i]);
2077                            } /* end of component loop i */
2078                        } /* end of k0 loop */
2079                    } /* end of k1 loop */
2080                } /* end of face 5 */
2081                /* GENERATOR SNIP_INTERPOLATE_REDUCED_FACES BOTTOM */
2082            } // end of parallel section
2083        } else {
2084            out.requireWrite();
2085            const double c0 = 0.044658198738520451079;
2086            const double c1 = 0.16666666666666666667;
2087            const double c2 = 0.62200846792814621559;
2088    #pragma omp parallel
2089            {
2090                /*** GENERATOR SNIP_INTERPOLATE_FACES TOP */
2091                if (m_faceOffset[0] > -1) {
2092    #pragma omp for nowait
2093                    for (index_t k2=0; k2 < m_NE2; ++k2) {
2094                        for (index_t k1=0; k1 < m_NE1; ++k1) {
2095                            const register double* f_000 = in.getSampleDataRO(INDEX3(0,k1,k2, m_N0,m_N1));
2096                            const register double* f_001 = in.getSampleDataRO(INDEX3(0,k1,k2+1, m_N0,m_N1));
2097                            const register double* f_011 = in.getSampleDataRO(INDEX3(0,k1+1,k2+1, m_N0,m_N1));
2098                            const register double* f_010 = in.getSampleDataRO(INDEX3(0,k1+1,k2, m_N0,m_N1));
2099                            double* o = out.getSampleDataRW(m_faceOffset[0]+INDEX2(k1,k2,m_NE1));
2100                            for (index_t i=0; i < numComp; ++i) {
2101                                o[INDEX2(i,numComp,0)] = f_000[i]*c2 + f_011[i]*c0 + c1*(f_001[i] + f_010[i]);
2102                                o[INDEX2(i,numComp,1)] = f_001[i]*c0 + f_010[i]*c2 + c1*(f_000[i] + f_011[i]);
2103                                o[INDEX2(i,numComp,2)] = f_001[i]*c2 + f_010[i]*c0 + c1*(f_000[i] + f_011[i]);
2104                                o[INDEX2(i,numComp,3)] = f_000[i]*c0 + f_011[i]*c2 + c1*(f_001[i] + f_010[i]);
2105                            } /* end of component loop i */
2106                        } /* end of k1 loop */
2107                    } /* end of k2 loop */
2108                } /* end of face 0 */
2109                if (m_faceOffset[1] > -1) {
2110    #pragma omp for nowait
2111                    for (index_t k2=0; k2 < m_NE2; ++k2) {
2112                        for (index_t k1=0; k1 < m_NE1; ++k1) {
2113                            const register double* f_101 = in.getSampleDataRO(INDEX3(m_N0-1,k1,k2+1, m_N0,m_N1));
2114                            const register double* f_100 = in.getSampleDataRO(INDEX3(m_N0-1,k1,k2, m_N0,m_N1));
2115                            const register double* f_110 = in.getSampleDataRO(INDEX3(m_N0-1,k1+1,k2, m_N0,m_N1));
2116                            const register double* f_111 = in.getSampleDataRO(INDEX3(m_N0-1,k1+1,k2+1, m_N0,m_N1));
2117                            double* o = out.getSampleDataRW(m_faceOffset[1]+INDEX2(k1,k2,m_NE1));
2118                            for (index_t i=0; i < numComp; ++i) {
2119                                o[INDEX2(i,numComp,0)] = f_100[i]*c2 + f_111[i]*c0 + c1*(f_101[i] + f_110[i]);
2120                                o[INDEX2(i,numComp,1)] = f_101[i]*c0 + f_110[i]*c2 + c1*(f_100[i] + f_111[i]);
2121                                o[INDEX2(i,numComp,2)] = f_101[i]*c2 + f_110[i]*c0 + c1*(f_100[i] + f_111[i]);
2122                                o[INDEX2(i,numComp,3)] = f_100[i]*c0 + f_111[i]*c2 + c1*(f_101[i] + f_110[i]);
2123                            } /* end of component loop i */
2124                        } /* end of k1 loop */
2125                    } /* end of k2 loop */
2126                } /* end of face 1 */
2127                if (m_faceOffset[2] > -1) {
2128    #pragma omp for nowait
2129                    for (index_t k2=0; k2 < m_NE2; ++k2) {
2130                        for (index_t k0=0; k0 < m_NE0; ++k0) {
2131                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,0,k2, m_N0,m_N1));
2132                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,0,k2+1, m_N0,m_N1));
2133                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,0,k2+1, m_N0,m_N1));
2134                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,0,k2, m_N0,m_N1));
2135                            double* o = out.getSampleDataRW(m_faceOffset[2]+INDEX2(k0,k2,m_NE0));
2136                            for (index_t i=0; i < numComp; ++i) {
2137                                o[INDEX2(i,numComp,0)] = f_000[i]*c2 + f_101[i]*c0 + c1*(f_001[i] + f_100[i]);
2138                                o[INDEX2(i,numComp,1)] = f_001[i]*c0 + f_100[i]*c2 + c1*(f_000[i] + f_101[i]);
2139                                o[INDEX2(i,numComp,2)] = f_001[i]*c2 + f_100[i]*c0 + c1*(f_000[i] + f_101[i]);
2140                                o[INDEX2(i,numComp,3)] = f_000[i]*c0 + f_101[i]*c2 + c1*(f_001[i] + f_100[i]);
2141                            } /* end of component loop i */
2142                        } /* end of k0 loop */
2143                    } /* end of k2 loop */
2144                } /* end of face 2 */
2145                if (m_faceOffset[3] > -1) {
2146    #pragma omp for nowait
2147                    for (index_t k2=0; k2 < m_NE2; ++k2) {
2148                        for (index_t k0=0; k0 < m_NE0; ++k0) {
2149                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,m_N1-1,k2, m_N0,m_N1));
2150                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,m_N1-1,k2+1, m_N0,m_N1));
2151                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,m_N1-1,k2, m_N0,m_N1));
2152                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,m_N1-1,k2+1, m_N0,m_N1));
2153                            double* o = out.getSampleDataRW(m_faceOffset[3]+INDEX2(k0,k2,m_NE0));
2154                            for (index_t i=0; i < numComp; ++i) {
2155                                o[INDEX2(i,numComp,0)] = f_010[i]*c2 + f_111[i]*c0 + c1*(f_011[i] + f_110[i]);
2156                                o[INDEX2(i,numComp,1)] = f_011[i]*c0 + f_110[i]*c2 + c1*(f_010[i] + f_111[i]);
2157                                o[INDEX2(i,numComp,2)] = f_011[i]*c2 + f_110[i]*c0 + c1*(f_010[i] + f_111[i]);
2158                                o[INDEX2(i,numComp,3)] = f_010[i]*c0 + f_111[i]*c2 + c1*(f_011[i] + f_110[i]);
2159                            } /* end of component loop i */
2160                        } /* end of k0 loop */
2161                    } /* end of k2 loop */
2162                } /* end of face 3 */
2163                if (m_faceOffset[4] > -1) {
2164    #pragma omp for nowait
2165                    for (index_t k1=0; k1 < m_NE1; ++k1) {
2166                        for (index_t k0=0; k0 < m_NE0; ++k0) {
2167                            const register double* f_000 = in.getSampleDataRO(INDEX3(k0,k1,0, m_N0,m_N1));
2168                            const register double* f_100 = in.getSampleDataRO(INDEX3(k0+1,k1,0, m_N0,m_N1));
2169                            const register double* f_110 = in.getSampleDataRO(INDEX3(k0+1,k1+1,0, m_N0,m_N1));
2170                            const register double* f_010 = in.getSampleDataRO(INDEX3(k0,k1+1,0, m_N0,m_N1));
2171                            double* o = out.getSampleDataRW(m_faceOffset[4]+INDEX2(k0,k1,m_NE0));
2172                            for (index_t i=0; i < numComp; ++i) {
2173                                o[INDEX2(i,numComp,0)] = f_000[i]*c2 + f_110[i]*c0 + c1*(f_010[i] + f_100[i]);
2174                                o[INDEX2(i,numComp,1)] = f_010[i]*c0 + f_100[i]*c2 + c1*(f_000[i] + f_110[i]);
2175                                o[INDEX2(i,numComp,2)] = f_010[i]*c2 + f_100[i]*c0 + c1*(f_000[i] + f_110[i]);
2176                                o[INDEX2(i,numComp,3)] = f_000[i]*c0 + f_110[i]*c2 + c1*(f_010[i] + f_100[i]);
2177                            } /* end of component loop i */
2178                        } /* end of k0 loop */
2179                    } /* end of k1 loop */
2180                } /* end of face 4 */
2181                if (m_faceOffset[5] > -1) {
2182    #pragma omp for nowait
2183                    for (index_t k1=0; k1 < m_NE1; ++k1) {
2184                        for (index_t k0=0; k0 < m_NE0; ++k0) {
2185                            const register double* f_001 = in.getSampleDataRO(INDEX3(k0,k1,m_N2-1, m_N0,m_N1));
2186                            const register double* f_101 = in.getSampleDataRO(INDEX3(k0+1,k1,m_N2-1, m_N0,m_N1));
2187                            const register double* f_011 = in.getSampleDataRO(INDEX3(k0,k1+1,m_N2-1, m_N0,m_N1));
2188                            const register double* f_111 = in.getSampleDataRO(INDEX3(k0+1,k1+1,m_N2-1, m_N0,m_N1));
2189                            double* o = out.getSampleDataRW(m_faceOffset[5]+INDEX2(k0,k1,m_NE0));
2190                            for (index_t i=0; i < numComp; ++i) {
2191                                o[INDEX2(i,numComp,0)] = f_001[i]*c2 + f_111[i]*c0 + c1*(f_011[i] + f_101[i]);
2192                                o[INDEX2(i,numComp,1)] = f_011[i]*c0 + f_101[i]*c2 + c1*(f_001[i] + f_111[i]);
2193                                o[INDEX2(i,numComp,2)] = f_011[i]*c2 + f_101[i]*c0 + c1*(f_001[i] + f_111[i]);
2194                                o[INDEX2(i,numComp,3)] = f_001[i]*c0 + f_111[i]*c2 + c1*(f_011[i] + f_101[i]);
2195                            } /* end of component loop i */
2196                        } /* end of k0 loop */
2197                    } /* end of k1 loop */
2198                } /* end of face 5 */
2199                /* GENERATOR SNIP_INTERPOLATE_FACES BOTTOM */
2200            } // end of parallel section
2201        }
2202  }  }
2203    
2204  //protected  //protected
2205  void Brick::interpolateNodesOnFaces(escript::Data& out, escript::Data& in) const  void Brick::assemblePDESingle(Paso_SystemMatrix* mat, escript::Data& rhs,
2206            const escript::Data& A, const escript::Data& B,
2207            const escript::Data& C, const escript::Data& D,
2208            const escript::Data& X, const escript::Data& Y,
2209            const escript::Data& d, const escript::Data& y) const
2210  {  {
2211      throw RipleyException("interpolateNodesOnFaces() not implemented");      const double h0 = m_l0/m_gNE0;
2212        const double h1 = m_l1/m_gNE1;
2213        const double h2 = m_l2/m_gNE2;
2214        /* GENERATOR SNIP_PDE_SINGLE_PRE TOP */
2215        const double w0 = 0.0009303791403858427308*h1*h2/h0;
2216        const double w1 = 0.0009303791403858427308*h2;
2217        const double w10 = 0.012958509748503046158*h0*h2/h1;
2218        const double w100 = 0.038141762351741127649*h0*h1;
2219        const double w101 = 0.000052682092703316795705*h0*h1;
2220        const double w102 = 0.0007337668937680108255*h0*h1;
2221        const double w103 = 0.010220054420048834761*h0*h1;
2222        const double w104 = -0.0001966122466178319053*h1*h2;
2223        const double w105 = -0.0001966122466178319053*h0*h2;
2224        const double w106 = -0.0007337668937680108255*h1*h2;
2225        const double w107 = -0.0007337668937680108255*h0*h2;
2226        const double w108 = -0.0027384553284542113967*h1*h2;
2227        const double w109 = -0.0027384553284542113967*h0*h2;
2228        const double w11 = -0.0034722222222222222222*h0;
2229        const double w110 = -0.010220054420048834761*h1*h2;
2230        const double w111 = -0.010220054420048834761*h0*h2;
2231        const double w112 = -0.0007337668937680108255*h0*h1;
2232        const double w113 = -0.010220054420048834761*h0*h1;
2233        const double w114 = -0.038141762351741127649*h0*h2;
2234        const double w115 = -0.000052682092703316795705*h0*h2;
2235        const double w116 = -0.0001966122466178319053*h0*h1;
2236        const double w117 = -0.0027384553284542113967*h0*h1;
2237        const double w118 = 0.000052682092703316795705*h0*h2;
2238        const double w119 = 0.038141762351741127649*h0*h2;
2239        const double w12 = 0.0034722222222222222222*h1;
2240        const double w120 = 0.000052682092703316795705*h1*h2;
2241        const double w121 = 0.038141762351741127649*h1*h2;
2242        const double w122 = -0.000052682092703316795705*h0*h1;
2243        const double w123 = -0.038141762351741127649*h0*h1;
2244        const double w124 = -0.000052682092703316795705*h1*h2;
2245        const double w125 = -0.038141762351741127649*h1*h2;
2246        const double w126 = 0.027777777777777777778*h1*h2;
2247        const double w127 = 0.027777777777777777778*h0*h2;
2248        const double w128 = 0.055555555555555555556*h0*h1;
2249        const double w129 = -0.027777777777777777778*h1*h2;
2250        const double w13 = 0.012958509748503046158*h0;
2251        const double w130 = -0.027777777777777777778*h0*h2;
2252        const double w131 = 0.013888888888888888889*h0*h1;
2253        const double w132 = -0.055555555555555555556*h0*h2;
2254        const double w133 = -0.027777777777777777778*h0*h1;
2255        const double w134 = 0.055555555555555555556*h0*h2;
2256        const double w135 = 0.027777777777777777778*h0*h1;
2257        const double w136 = -0.013888888888888888889*h0*h1;
2258        const double w137 = 0.055555555555555555556*h1*h2;
2259        const double w138 = -0.013888888888888888889*h1*h2;
2260        const double w139 = -0.013888888888888888889*h0*h2;
2261        const double w14 = -0.0034722222222222222222*h0*h1/h2;
2262        const double w140 = -0.055555555555555555556*h0*h1;
2263        const double w141 = 0.013888888888888888889*h1*h2;
2264        const double w142 = 0.013888888888888888889*h0*h2;
2265        const double w143 = -0.055555555555555555556*h1*h2;
2266        const double w144 = 0.000041549056553524783501*h0*h1*h2;
2267        const double w145 = 0.0005787037037037037037*h0*h1*h2;
2268        const double w146 = 0.0080603027952983270684*h0*h1*h2;
2269        const double w147 = 0.0001550631900643071218*h0*h1*h2;
2270        const double w148 = 0.002159751624750507693*h0*h1*h2;
2271        const double w149 = 0.03008145955644280058*h0*h1*h2;
2272        const double w15 = 0.012958509748503046158*h1*h2/h0;
2273        const double w150 = 0.000011133036149792012204*h0*h1*h2;
2274        const double w151 = 0.018518518518518518519*h0*h1*h2;
2275        const double w152 = 0.0092592592592592592592*h0*h1*h2;
2276        const double w153 = 0.0046296296296296296296*h0*h1*h2;
2277        const double w154 = 0.037037037037037037037*h0*h1*h2;
2278        const double w155 = -0.077751058491018276949*h1*h2;
2279        const double w156 = -0.077751058491018276949*h0*h2;
2280        const double w157 = -0.077751058491018276949*h0*h1;
2281        const double w158 = -0.020833333333333333333*h0*h2;
2282        const double w159 = -0.020833333333333333333*h0*h1;
2283        const double w16 = -0.0034722222222222222222*h1;
2284        const double w160 = -0.020833333333333333333*h1*h2;
2285        const double w161 = -0.0055822748423150563848*h0*h1;
2286        const double w162 = -0.0055822748423150563848*h0*h2;
2287        const double w163 = -0.0055822748423150563848*h1*h2;
2288        const double w164 = 0.077751058491018276949*h1*h2;
2289        const double w165 = 0.020833333333333333333*h1*h2;
2290        const double w166 = 0.0055822748423150563848*h1*h2;
2291        const double w167 = 0.077751058491018276949*h0*h2;
2292        const double w168 = 0.020833333333333333333*h0*h2;
2293        const double w169 = 0.0055822748423150563848*h0*h2;
2294        const double w17 = -0.0009303791403858427308*h0;
2295        const double w170 = 0.077751058491018276949*h0*h1;
2296        const double w171 = 0.020833333333333333333*h0*h1;
2297        const double w172 = 0.0055822748423150563848*h0*h1;
2298        const double w173 = -0.25*h1*h2;
2299        const double w174 = -0.25*h0*h2;
2300        const double w175 = -0.25*h0*h1;
2301        const double w176 = 0.25*h1*h2;
2302        const double w177 = 0.25*h0*h2;
2303        const double w178 = 0.25*h0*h1;
2304        const double w179 = 0.061320326520293008568*h0*h1*h2;
2305        const double w18 = 0.012958509748503046158*h1;
2306        const double w180 = 0.01643073197072526838*h0*h1*h2;
2307        const double w181 = 0.004402601362608064953*h0*h1*h2;
2308        const double w182 = 0.0011796734797069914318*h0*h1*h2;
2309        const double w183 = 0.125*h0*h1*h2;
2310        const double w19 = 0.0034722222222222222222*h0;
2311        const double w2 = -0.00024929433932114870101*h1;
2312        const double w20 = 0.012958509748503046158*h2;
2313        const double w21 = -0.012958509748503046158*h1;
2314        const double w22 = -0.012958509748503046158*h0;
2315        const double w23 = 0.04836181677178996241*h1;
2316        const double w24 = 0.04836181677178996241*h0;
2317        const double w25 = -0.04836181677178996241*h0*h1/h2;
2318        const double w26 = 0.00024929433932114870101*h1;
2319        const double w27 = 0.00024929433932114870101*h0;
2320        const double w28 = -0.04836181677178996241*h1;
2321        const double w29 = -0.04836181677178996241*h0;
2322        const double w3 = 0.0009303791403858427308*h0*h2/h1;
2323        const double w30 = -0.0009303791403858427308*h1*h2/h0;
2324        const double w31 = -0.0009303791403858427308*h2;
2325        const double w32 = -0.0009303791403858427308*h0*h2/h1;
2326        const double w33 = 0.0034722222222222222222*h0*h1/h2;
2327        const double w34 = -0.0034722222222222222222*h2;
2328        const double w35 = -0.00024929433932114870101*h2;
2329        const double w36 = -0.012958509748503046158*h1*h2/h0;
2330        const double w37 = -0.012958509748503046158*h2;
2331        const double w38 = -0.012958509748503046158*h0*h2/h1;
2332        const double w39 = -0.04836181677178996241*h2;
2333        const double w4 = -0.00024929433932114870101*h0;
2334        const double w40 = -0.0034722222222222222222*h0*h2/h1;
2335        const double w41 = 0.0009303791403858427308*h0*h1/h2;
2336        const double w42 = 0.04836181677178996241*h2;
2337        const double w43 = -0.04836181677178996241*h0*h2/h1;
2338        const double w44 = 0.012958509748503046158*h0*h1/h2;
2339        const double w45 = -0.00024929433932114870101*h0*h2/h1;
2340        const double w46 = 0.00024929433932114870101*h2;
2341        const double w47 = -0.0034722222222222222222*h1*h2/h0;
2342        const double w48 = -0.00024929433932114870101*h1*h2/h0;
2343        const double w49 = -0.04836181677178996241*h1*h2/h0;
2344        const double w5 = 0.0009303791403858427308*h1;
2345        const double w50 = 0.0034722222222222222222*h0*h2/h1;
2346        const double w51 = -0.0009303791403858427308*h0*h1/h2;
2347        const double w52 = -0.012958509748503046158*h0*h1/h2;
2348        const double w53 = 0.0034722222222222222222*h1*h2/h0;
2349        const double w54 = 0.00024929433932114870101*h0*h1/h2;
2350        const double w55 = 0.04836181677178996241*h0*h2/h1;
2351        const double w56 = 0.04836181677178996241*h1*h2/h0;
2352        const double w57 = 0.04836181677178996241*h0*h1/h2;
2353        const double w58 = 0.00024929433932114870101*h1*h2/h0;
2354        const double w59 = 0.00024929433932114870101*h0*h2/h1;
2355        const double w6 = 0.0009303791403858427308*h0;
2356        const double w60 = 0.055555555555555555556*h1*h2/h0;
2357        const double w61 = 0.041666666666666666667*h2;
2358        const double w62 = -0.083333333333333333333*h1;
2359        const double w63 = 0.055555555555555555556*h0*h2/h1;
2360        const double w64 = -0.083333333333333333333*h0;
2361        const double w65 = 0.083333333333333333333*h1;
2362        const double w66 = 0.083333333333333333333*h0;
2363        const double w67 = -0.11111111111111111111*h0*h1/h2;
2364        const double w68 = -0.055555555555555555556*h1*h2/h0;
2365        const double w69 = -0.083333333333333333333*h2;
2366        const double w7 = -0.00024929433932114870101*h0*h1/h2;
2367        const double w70 = -0.041666666666666666667*h1;
2368        const double w71 = -0.055555555555555555556*h0*h2/h1;
2369        const double w72 = -0.041666666666666666667*h0;
2370        const double w73 = 0.041666666666666666667*h1;
2371        const double w74 = 0.041666666666666666667*h0;
2372        const double w75 = 0.027777777777777777778*h0*h1/h2;
2373        const double w76 = 0.083333333333333333333*h2;
2374        const double w77 = -0.11111111111111111111*h0*h2/h1;
2375        const double w78 = 0.055555555555555555556*h0*h1/h2;
2376        const double w79 = -0.11111111111111111111*h1*h2/h0;
2377        const double w8 = 0.0034722222222222222222*h2;
2378        const double w80 = -0.027777777777777777778*h1*h2/h0;
2379        const double w81 = -0.041666666666666666667*h2;
2380        const double w82 = -0.027777777777777777778*h0*h2/h1;
2381        const double w83 = -0.027777777777777777778*h0*h1/h2;
2382        const double w84 = 0.027777777777777777778*h0*h2/h1;
2383        const double w85 = -0.055555555555555555556*h0*h1/h2;
2384        const double w86 = 0.11111111111111111111*h1*h2/h0;
2385        const double w87 = 0.11111111111111111111*h0*h2/h1;
2386        const double w88 = 0.11111111111111111111*h0*h1/h2;
2387        const double w89 = 0.027777777777777777778*h1*h2/h0;
2388        const double w9 = -0.0009303791403858427308*h1;
2389        const double w90 = 0.0001966122466178319053*h1*h2;
2390        const double w91 = 0.0001966122466178319053*h0*h2;
2391        const double w92 = 0.0001966122466178319053*h0*h1;
2392        const double w93 = 0.0007337668937680108255*h1*h2;
2393        const double w94 = 0.0027384553284542113967*h0*h2;
2394        const double w95 = 0.0027384553284542113967*h0*h1;
2395        const double w96 = 0.0027384553284542113967*h1*h2;
2396        const double w97 = 0.0007337668937680108255*h0*h2;
2397        const double w98 = 0.010220054420048834761*h1*h2;
2398        const double w99 = 0.010220054420048834761*h0*h2;
2399        /* GENERATOR SNIP_PDE_SINGLE_PRE BOTTOM */
2400    
2401        rhs.requireWrite();
2402    #pragma omp parallel
2403        {
2404            for (index_t k2_0=0; k2_0<2; k2_0++) { // colouring
2405    #pragma omp for
2406                for (index_t k2=k2_0; k2<m_NE2; k2+=2) {
2407                    for (index_t k1=0; k1<m_NE1; ++k1) {
2408                        for (index_t k0=0; k0<m_NE0; ++k0)  {
2409                            bool add_EM_S=false;
2410                            bool add_EM_F=false;
2411                            vector<double> EM_S(8*8, 0);
2412                            vector<double> EM_F(8, 0);
2413                            const index_t e = k0 + m_NE0*k1 + m_NE0*m_NE1*k2;
2414                            /* GENERATOR SNIP_PDE_SINGLE TOP */
2415                            ///////////////
2416                            // process A //
2417                            ///////////////
2418                            if (!A.isEmpty()) {
2419                                add_EM_S=true;
2420                                const double* A_p=const_cast<escript::Data*>(&A)->getSampleDataRO(e);
2421                                if (A.actsExpanded()) {
2422                                    const register double A_00_0 = A_p[INDEX3(0,0,0,3,3)];
2423                                    const register double A_01_0 = A_p[INDEX3(0,1,0,3,3)];
2424                                    const register double A_02_0 = A_p[INDEX3(0,2,0,3,3)];
2425                                    const register double A_10_0 = A_p[INDEX3(1,0,0,3,3)];
2426                                    const register double A_11_0 = A_p[INDEX3(1,1,0,3,3)];
2427                                    const register double A_12_0 = A_p[INDEX3(1,2,0,3,3)];
2428                                    const register double A_20_0 = A_p[INDEX3(2,0,0,3,3)];
2429                                    const register double A_21_0 = A_p[INDEX3(2,1,0,3,3)];
2430                                    const register double A_22_0 = A_p[INDEX3(2,2,0,3,3)];
2431                                    const register double A_00_1 = A_p[INDEX3(0,0,1,3,3)];
2432                                    const register double A_01_1 = A_p[INDEX3(0,1,1,3,3)];
2433                                    const register double A_02_1 = A_p[INDEX3(0,2,1,3,3)];
2434                                    const register double A_10_1 = A_p[INDEX3(1,0,1,3,3)];
2435                                    const register double A_11_1 = A_p[INDEX3(1,1,1,3,3)];
2436                                    const register double A_12_1 = A_p[INDEX3(1,2,1,3,3)];
2437                                    const register double A_20_1 = A_p[INDEX3(2,0,1,3,3)];
2438                                    const register double A_21_1 = A_p[INDEX3(2,1,1,3,3)];
2439                                    const register double A_22_1 = A_p[INDEX3(2,2,1,3,3)];
2440                                    const register double A_00_2 = A_p[INDEX3(0,0,2,3,3)];
2441                                    const register double A_01_2 = A_p[INDEX3(0,1,2,3,3)];
2442                                    const register double A_02_2 = A_p[INDEX3(0,2,2,3,3)];
2443                                    const register double A_10_2 = A_p[INDEX3(1,0,2,3,3)];
2444                                    const register double A_11_2 = A_p[INDEX3(1,1,2,3,3)];
2445                                    const register double A_12_2 = A_p[INDEX3(1,2,2,3,3)];
2446                                    const register double A_20_2 = A_p[INDEX3(2,0,2,3,3)];
2447                                    const register double A_21_2 = A_p[INDEX3(2,1,2,3,3)];
2448                                    const register double A_22_2 = A_p[INDEX3(2,2,2,3,3)];
2449                                    const register double A_00_3 = A_p[INDEX3(0,0,3,3,3)];
2450                                    const register double A_01_3 = A_p[INDEX3(0,1,3,3,3)];
2451                                    const register double A_02_3 = A_p[INDEX3(0,2,3,3,3)];
2452                                    const register double A_10_3 = A_p[INDEX3(1,0,3,3,3)];
2453                                    const register double A_11_3 = A_p[INDEX3(1,1,3,3,3)];
2454                                    const register double A_12_3 = A_p[INDEX3(1,2,3,3,3)];
2455                                    const register double A_20_3 = A_p[INDEX3(2,0,3,3,3)];
2456                                    const register double A_21_3 = A_p[INDEX3(2,1,3,3,3)];
2457                                    const register double A_22_3 = A_p[INDEX3(2,2,3,3,3)];
2458                                    const register double A_00_4 = A_p[INDEX3(0,0,4,3,3)];
2459                                    const register double A_01_4 = A_p[INDEX3(0,1,4,3,3)];
2460                                    const register double A_02_4 = A_p[INDEX3(0,2,4,3,3)];
2461                                    const register double A_10_4 = A_p[INDEX3(1,0,4,3,3)];
2462                                    const register double A_11_4 = A_p[INDEX3(1,1,4,3,3)];
2463                                    const register double A_12_4 = A_p[INDEX3(1,2,4,3,3)];
2464                                    const register double A_20_4 = A_p[INDEX3(2,0,4,3,3)];
2465                                    const register double A_21_4 = A_p[INDEX3(2,1,4,3,3)];
2466                                    const register double A_22_4 = A_p[INDEX3(2,2,4,3,3)];
2467                                    const register double A_00_5 = A_p[INDEX3(0,0,5,3,3)];
2468                                    const register double A_01_5 = A_p[INDEX3(0,1,5,3,3)];
2469                                    const register double A_02_5 = A_p[INDEX3(0,2,5,3,3)];
2470                                    const register double A_10_5 = A_p[INDEX3(1,0,5,3,3)];
2471                                    const register double A_11_5 = A_p[INDEX3(1,1,5,3,3)];
2472                                    const register double A_12_5 = A_p[INDEX3(1,2,5,3,3)];
2473                                    const register double A_20_5 = A_p[INDEX3(2,0,5,3,3)];
2474                                    const register double A_21_5 = A_p[INDEX3(2,1,5,3,3)];
2475                                    const register double A_22_5 = A_p[INDEX3(2,2,5,3,3)];
2476                                    const register double A_00_6 = A_p[INDEX3(0,0,6,3,3)];
2477                                    const register double A_01_6 = A_p[INDEX3(0,1,6,3,3)];
2478                                    const register double A_02_6 = A_p[INDEX3(0,2,6,3,3)];
2479                                    const register double A_10_6 = A_p[INDEX3(1,0,6,3,3)];
2480                                    const register double A_11_6 = A_p[INDEX3(1,1,6,3,3)];
2481                                    const register double A_12_6 = A_p[INDEX3(1,2,6,3,3)];
2482                                    const register double A_20_6 = A_p[INDEX3(2,0,6,3,3)];
2483                                    const register double A_21_6 = A_p[INDEX3(2,1,6,3,3)];
2484                                    const register double A_22_6 = A_p[INDEX3(2,2,6,3,3)];
2485                                    const register double A_00_7 = A_p[INDEX3(0,0,7,3,3)];
2486                                    const register double A_01_7 = A_p[INDEX3(0,1,7,3,3)];
2487                                    const register double A_02_7 = A_p[INDEX3(0,2,7,3,3)];
2488                                    const register double A_10_7 = A_p[INDEX3(1,0,7,3,3)];
2489                                    const register double A_11_7 = A_p[INDEX3(1,1,7,3,3)];
2490                                    const register double A_12_7 = A_p[INDEX3(1,2,7,3,3)];
2491                                    const register double A_20_7 = A_p[INDEX3(2,0,7,3,3)];
2492                                    const register double A_21_7 = A_p[INDEX3(2,1,7,3,3)];
2493                                    const register double A_22_7 = A_p[INDEX3(2,2,7,3,3)];
2494                                    const register double tmp160_0 = A_12_0 + A_12_6 + A_21_0 + A_21_6;
2495                                    const register double tmp8_0 = A_21_0 + A_21_6;
2496                                    const register double tmp135_0 = A_10_1 + A_10_2 + A_10_5 + A_10_6;
2497                                    const register double tmp67_0 = A_02_2 + A_02_7;
2498                                    const register double tmp211_0 = A_12_6 + A_21_6;
2499                                    const register double tmp180_0 = A_10_2 + A_10_6;
2500                                    const register double tmp37_0 = A_00_0 + A_00_1 + A_00_2 + A_00_3;
2501                                    const register double tmp92_0 = A_11_0 + A_11_1 + A_11_2 + A_11_3 + A_11_4 + A_11_5 + A_11_6 + A_11_7;
2502                                    const register double tmp195_0 = A_02_2 + A_20_2;
2503                                    const register double tmp70_0 = A_01_0 + A_01_7;
2504                                    const register double tmp139_0 = A_02_3 + A_02_4 + A_20_1 + A_20_6;
2505                                    const register double tmp200_0 = A_12_3 + A_12_5 + A_21_3 + A_21_5;
2506                                    const register double tmp60_0 = A_22_0 + A_22_2 + A_22_4 + A_22_6;
2507                                    const register double tmp192_0 = A_01_5 + A_10_5;
2508                                    const register double tmp46_0 = A_21_0 + A_21_7;
2509                                    const register double tmp48_0 = A_10_0 + A_10_7;
2510                                    const register double tmp166_0 = A_11_5 + A_11_7;
2511                                    const register double tmp221_0 = A_02_1 + A_02_6 + A_20_3 + A_20_4;
2512                                    const register double tmp50_0 = A_02_4 + A_02_6 + A_20_4 + A_20_6;
2513                                    const register double tmp217_0 = A_02_3 + A_02_4 + A_20_3 + A_20_4;
2514                                    const register double tmp216_0 = A_01_2 + A_01_5 + A_10_2 + A_10_5;
2515                                    const register double tmp104_0 = A_22_2 + A_22_6;
2516                                    const register double tmp72_0 = A_20_3 + A_20_6;
2517                                    const register double tmp79_0 = A_10_4 + A_10_7;
2518                                    const register double tmp86_0 = A_01_2 + A_01_6 + A_10_1 + A_10_5;
2519                                    const register double tmp214_0 = A_12_0 + A_12_7 + A_21_0 + A_21_7;
2520                                    const register double tmp32_0 = A_02_0 + A_02_2;
2521                                    const register double tmp112_0 = A_01_0 + A_01_4 + A_10_3 + A_10_7;
2522                                    const register double tmp197_0 = A_12_0 + A_21_0;
2523                                    const register double tmp106_0 = A_22_1 + A_22_5;
2524                                    const register double tmp2_0 = A_00_0 + A_00_1 + A_00_4 + A_00_5;
2525                                    const register double tmp115_0 = A_02_5 + A_02_7 + A_20_0 + A_20_2;
2526                                    const register double tmp175_0 = A_01_3 + A_01_7;
2527                                    const register double tmp126_0 = A_01_2 + A_01_5 + A_10_1 + A_10_6;
2528                                    const register double tmp90_0 = A_00_0 + A_00_1 + A_00_2 + A_00_3 + A_00_4 + A_00_5 + A_00_6 + A_00_7;
2529                                    const register double tmp47_0 = A_12_0 + A_12_6;
2530                                    const register double tmp205_0 = A_02_7 + A_20_7;
2531                                    const register double tmp148_0 = A_01_3 + A_01_4;
2532                                    const register double tmp113_0 = A_01_3 + A_01_7 + A_10_0 + A_10_4;
2533                                    const register double tmp43_0 = A_20_4 + A_20_6;
2534                                    const register double tmp161_0 = A_02_1 + A_02_6 + A_20_1 + A_20_6;
2535                                    const register double tmp69_0 = A_12_0 + A_12_1 + A_12_6 + A_12_7 + A_21_0 + A_21_1 + A_21_6 + A_21_7;
2536                                    const register double tmp176_0 = A_01_1 + A_01_2 + A_01_5 + A_01_6;
2537                                    const register double tmp105_0 = A_01_2 + A_01_6 + A_10_2 + A_10_6;
2538                                    const register double tmp22_0 = A_01_5 + A_10_6;
2539                                    const register double tmp91_0 = A_02_4 + A_02_6 + A_20_1 + A_20_3;
2540                                    const register double tmp206_0 = A_12_7 + A_21_7;
2541                                    const register double tmp188_0 = A_02_5 + A_20_5;
2542                                    const register double tmp117_0 = A_21_1 + A_21_6;
2543                                    const register double tmp165_0 = A_01_1 + A_01_6;
2544                                    const register double tmp66_0 = A_00_4 + A_00_5;
2545                                    const register double tmp57_0 = A_02_0 + A_02_2 + A_02_5 + A_02_7 + A_20_0 + A_20_2 + A_20_5 + A_20_7;
2546                                    const register double tmp31_0 = A_21_4 + A_21_5;
2547                                    const register double tmp3_0 = A_11_0 + A_11_2 + A_11_4 + A_11_6;
2548                                    const register double tmp183_0 = A_12_0 + A_12_7;
2549                                    const register double tmp61_0 = A_02_1 + A_02_3 + A_20_1 + A_20_3;
2550                                    const register double tmp54_0 = A_10_5 + A_10_6;
2551                                    const register double tmp18_0 = A_02_3 + A_02_6;
2552                                    const register double tmp119_0 = A_12_2 + A_12_3 + A_12_4 + A_12_5 + A_21_2 + A_21_3 + A_21_4 + A_21_5;
2553                                    const register double tmp29_0 = A_21_2 + A_21_3;
2554                                    const register double tmp17_0 = A_01_3 + A_01_7 + A_10_3 + A_10_7;
2555                                    const register double tmp212_0 = A_02_6 + A_20_6;
2556                                    const register double tmp220_0 = A_02_3 + A_20_6;
2557                                    const register double tmp78_0 = A_20_0 + A_20_7;
2558                                    const register double tmp215_0 = A_01_6 + A_10_6;
2559                                    const register double tmp203_0 = A_01_7 + A_10_7;
2560                                    const register double tmp87_0 = A_12_2 + A_12_3 + A_21_4 + A_21_5;
2561                                    const register double tmp114_0 = A_02_0 + A_02_2 + A_20_5 + A_20_7;
2562                                    const register double tmp0_0 = A_01_0 + A_01_4 + A_10_0 + A_10_4;
2563                                    const register double tmp202_0 = A_01_3 + A_01_4 + A_10_3 + A_10_4;
2564                                    const register double tmp4_0 = A_20_0 + A_20_5;
2565                                    const register double tmp65_0 = A_00_2 + A_00_3;
2566                                    const register double tmp24_0 = A_20_1 + A_20_3;
2567                                    const register double tmp64_0 = A_10_0 + A_10_3;
2568                                    const register double tmp170_0 = A_02_0 + A_02_2 + A_20_0 + A_20_2;
2569                                    const register double tmp11_0 = A_20_1 + A_20_6;
2570                                    const register double tmp82_0 = A_12_4 + A_12_5 + A_21_4 + A_21_5;
2571                                    const register double tmp99_0 = A_01_4 + A_10_7;
2572                                    const register double tmp49_0 = A_12_1 + A_12_7;
2573                                    const register double tmp130_0 = A_12_0 + A_12_1 + A_12_6 + A_12_7;
2574                                    const register double tmp144_0 = A_01_0 + A_10_3;
2575                                    const register double tmp109_0 = A_22_0 + A_22_3 + A_22_4 + A_22_7;
2576                                    const register double tmp185_0 = A_02_0 + A_02_7 + A_20_2 + A_20_5;
2577                                    const register double tmp157_0 = A_01_4 + A_10_4;
2578                                    const register double tmp51_0 = A_22_1 + A_22_3 + A_22_5 + A_22_7;
2579                                    const register double tmp146_0 = A_00_6 + A_00_7;
2580                                    const register double tmp147_0 = A_12_0 + A_12_1 + A_21_0 + A_21_1;
2581                                    const register double tmp150_0 = A_00_2 + A_00_3 + A_00_4 + A_00_5;
2582                                    const register double tmp62_0 = A_21_3 + A_21_5;
2583                                    const register double tmp223_0 = A_12_2 + A_21_4;
2584                                    const register double tmp16_0 = A_02_2 + A_02_5;
2585                                    const register double tmp168_0 = A_11_1 + A_11_3 + A_11_4 + A_11_6;
2586                                    const register double tmp88_0 = A_12_4 + A_12_5 + A_21_2 + A_21_3;
2587                                    const register double tmp142_0 = A_01_7 + A_10_4;
2588                                    const register double tmp34_0 = A_20_0 + A_20_2 + A_20_5 + A_20_7;
2589                                    const register double tmp71_0 = A_00_0 + A_00_1 + A_00_6 + A_00_7;
2590                                    const register double tmp213_0 = A_02_1 + A_20_1;
2591                                    const register double tmp227_0 = A_12_2 + A_12_5 + A_21_3 + A_21_4;
2592                                    const register double tmp228_0 = A_12_1 + A_21_7;
2593                                    const register double tmp140_0 = A_01_2 + A_01_6;
2594                                    const register double tmp74_0 = A_22_0 + A_22_1 + A_22_4 + A_22_5;
2595                                    const register double tmp167_0 = A_11_0 + A_11_2;
2596                                    const register double tmp143_0 = A_01_3 + A_01_4 + A_10_0 + A_10_7;
2597                                    const register double tmp83_0 = A_02_0 + A_02_5;
2598                                    const register double tmp14_0 = A_22_1 + A_22_2 + A_22_5 + A_22_6;
2599                                    const register double tmp5_0 = A_12_1 + A_12_6;
2600                                    const register double tmp94_0 = A_02_1 + A_02_3;
2601                                    const register double tmp193_0 = A_01_1 + A_01_6 + A_10_1 + A_10_6;
2602                                    const register double tmp97_0 = A_02_0 + A_02_2 + A_02_5 + A_02_7;
2603                                    const register double tmp131_0 = A_01_1 + A_01_5;
2604                                    const register double tmp124_0 = A_01_6 + A_10_5;
2605                                    const register double tmp149_0 = A_12_6 + A_12_7 + A_21_6 + A_21_7;
2606                                    const register double tmp187_0 = A_01_2 + A_10_2;
2607                                    const register double tmp93_0 = A_01_1 + A_01_2 + A_10_1 + A_10_2;
2608                                    const register double tmp25_0 = A_01_4 + A_01_7 + A_10_4 + A_10_7;
2609                                    const register double tmp156_0 = A_12_2 + A_12_5 + A_21_2 + A_21_5;
2610                                    const register double tmp20_0 = A_21_2 + A_21_5;
2611                                    const register double tmp55_0 = A_21_2 + A_21_4;
2612                                    const register double tmp208_0 = A_12_1 + A_12_6 + A_21_0 + A_21_7;
2613                                    const register double tmp125_0 = A_12_4 + A_12_5;
2614                                    const register double tmp158_0 = A_01_0 + A_01_7 + A_10_0 + A_10_7;
2615                                    const register double tmp108_0 = A_01_1 + A_01_5 + A_10_1 + A_10_5;
2616                                    const register double tmp199_0 = A_12_2 + A_12_4 + A_21_2 + A_21_4;
2617                                    const register double tmp10_0 = A_02_1 + A_02_4;
2618                                    const register double tmp182_0 = A_02_3 + A_02_6 + A_20_3 + A_20_6;
2619                                    const register double tmp132_0 = A_02_1 + A_20_4;
2620                                    const register double tmp191_0 = A_12_3 + A_12_4 + A_21_3 + A_21_4;
2621                                    const register double tmp35_0 = A_11_0 + A_11_1 + A_11_2 + A_11_3;
2622                                    const register double tmp164_0 = A_10_3 + A_10_4;
2623                                    const register double tmp190_0 = A_12_5 + A_21_5;
2624                                    const register double tmp73_0 = A_02_1 + A_02_6;
2625                                    const register double tmp98_0 = A_01_0 + A_01_7 + A_10_3 + A_10_4;
2626                                    const register double tmp225_0 = A_12_4 + A_21_2;
2627                                    const register double tmp103_0 = A_02_4 + A_02_6;
2628                                    const register double tmp194_0 = A_02_0 + A_02_7 + A_20_0 + A_20_7;
2629                                    const register double tmp207_0 = A_12_0 + A_21_6;
2630                                    const register double tmp102_0 = A_20_5 + A_20_7;
2631                                    const register double tmp1_0 = A_22_3 + A_22_7;
2632                                    const register double tmp172_0 = A_10_1 + A_10_5;
2633                                    const register double tmp222_0 = A_12_5 + A_21_3;
2634                                    const register double tmp201_0 = A_02_2 + A_02_5 + A_20_2 + A_20_5;
2635                                    const register double tmp155_0 = A_12_4 + A_21_4;
2636                                    const register double tmp174_0 = A_02_1 + A_02_4 + A_20_1 + A_20_4;
2637                                    const register double tmp59_0 = A_01_0 + A_01_3;
2638                                    const register double tmp21_0 = A_20_2 + A_20_7;
2639                                    const register double tmp141_0 = A_02_2 + A_02_7 + A_20_2 + A_20_7;
2640                                    const register double tmp210_0 = A_01_1 + A_10_1;
2641                                    const register double tmp145_0 = A_00_0 + A_00_1;
2642                                    const register double tmp121_0 = A_12_0 + A_12_1 + A_21_6 + A_21_7;
2643                                    const register double tmp224_0 = A_12_3 + A_12_4 + A_21_2 + A_21_5;
2644                                    const register double tmp186_0 = A_02_2 + A_20_7;
2645                                    const register double tmp53_0 = A_11_4 + A_11_6;
2646                                    const register double tmp184_0 = A_02_5 + A_20_0;
2647                                    const register double tmp38_0 = A_12_0 + A_12_1;
2648                                    const register double tmp12_0 = A_01_1 + A_01_2 + A_01_5 + A_01_6 + A_10_1 + A_10_2 + A_10_5 + A_10_6;
2649                                    const register double tmp230_0 = A_12_6 + A_21_0;
2650                                    const register double tmp23_0 = A_11_4 + A_11_5 + A_11_6 + A_11_7;
2651                                    const register double tmp81_0 = A_20_1 + A_20_4;
2652                                    const register double tmp134_0 = A_10_3 + A_10_7;
2653                                    const register double tmp129_0 = A_21_0 + A_21_1;
2654                                    const register double tmp137_0 = A_01_0 + A_01_3 + A_01_4 + A_01_7;
2655                                    const register double tmp198_0 = A_01_0 + A_10_0;
2656                                    const register double tmp9_0 = A_21_1 + A_21_7;
2657                                    const register double tmp179_0 = A_01_0 + A_01_4;
2658                                    const register double tmp100_0 = A_20_1 + A_20_3 + A_20_4 + A_20_6;
2659                                    const register double tmp173_0 = A_02_0 + A_20_5;
2660                                    const register double tmp42_0 = A_21_0 + A_21_1 + A_21_6 + A_21_7;
2661                                    const register double tmp226_0 = A_12_3 + A_21_5;
2662                                    const register double tmp6_0 = A_22_0 + A_22_4;
2663                                    const register double tmp218_0 = A_12_1 + A_21_1;
2664                                    const register double tmp28_0 = A_01_2 + A_10_1;
2665                                    const register double tmp133_0 = A_02_6 + A_20_3;
2666                                    const register double tmp13_0 = A_00_2 + A_00_3 + A_00_6 + A_00_7;
2667                                    const register double tmp27_0 = A_12_2 + A_12_3 + A_12_4 + A_12_5;
2668                                    const register double tmp75_0 = A_10_1 + A_10_6;
2669                                    const register double tmp36_0 = A_01_0 + A_01_3 + A_10_0 + A_10_3;
2670                                    const register double tmp138_0 = A_10_0 + A_10_4;
2671                                    const register double tmp189_0 = A_12_2 + A_21_2;
2672                                    const register double tmp181_0 = A_02_7 + A_20_2;
2673                                    const register double tmp85_0 = A_02_1 + A_02_3 + A_20_4 + A_20_6;
2674                                    const register double tmp122_0 = A_01_1 + A_10_2;
2675                                    const register double tmp95_0 = A_01_3 + A_10_0;
2676                                    const register double tmp120_0 = A_12_6 + A_12_7 + A_21_0 + A_21_1;
2677                                    const register double tmp196_0 = A_02_0 + A_20_0;
2678                                    const register double tmp171_0 = A_02_3 + A_02_4;
2679                                    const register double tmp204_0 = A_12_1 + A_12_6 + A_21_1 + A_21_6;
2680                                    const register double tmp45_0 = A_10_1 + A_10_2;
2681                                    const register double tmp101_0 = A_01_5 + A_01_6 + A_10_5 + A_10_6;
2682                                    const register double tmp58_0 = A_11_0 + A_11_2 + A_11_5 + A_11_7;
2683                                    const register double tmp107_0 = A_20_3 + A_20_4;
2684                                    const register double tmp30_0 = A_01_1 + A_01_6 + A_10_2 + A_10_5;
2685                                    const register double tmp63_0 = A_12_2 + A_12_5;
2686                                    const register double tmp127_0 = A_12_2 + A_12_3;
2687                                    const register double tmp177_0 = A_02_2 + A_02_5 + A_20_0 + A_20_7;
2688                                    const register double tmp178_0 = A_10_0 + A_10_3 + A_10_4 + A_10_7;
2689                                    const register double tmp76_0 = A_01_1 + A_01_2;
2690                                    const register double tmp80_0 = A_22_2 + A_22_3 + A_22_6 + A_22_7;
2691                                    const register double tmp41_0 = A_12_6 + A_12_7;
2692                                    const register double tmp89_0 = A_01_0 + A_01_3 + A_01_4 + A_01_7 + A_10_0 + A_10_3 + A_10_4 + A_10_7;
2693                                    const register double tmp116_0 = A_02_1 + A_02_3 + A_02_4 + A_02_6 + A_20_1 + A_20_3 + A_20_4 + A_20_6;
2694                                    const register double tmp33_0 = A_22_0 + A_22_1 + A_22_2 + A_22_3 + A_22_4 + A_22_5 + A_22_6 + A_22_7;
2695                                    const register double tmp169_0 = A_21_3 + A_21_4;
2696                                    const register double tmp96_0 = A_20_0 + A_20_2;
2697                                    const register double tmp111_0 = A_12_3 + A_12_4;
2698                                    const register double tmp118_0 = A_20_2 + A_20_5;
2699                                    const register double tmp19_0 = A_12_3 + A_12_5;
2700                                    const register double tmp68_0 = A_01_5 + A_01_6;
2701                                    const register double tmp7_0 = A_11_1 + A_11_3 + A_11_5 + A_11_7;
2702                                    const register double tmp154_0 = A_12_3 + A_21_3;
2703                                    const register double tmp152_0 = A_02_4 + A_20_4;
2704                                    const register double tmp153_0 = A_02_3 + A_20_3;
2705                                    const register double tmp163_0 = A_02_5 + A_02_7 + A_20_5 + A_20_7;
2706                                    const register double tmp44_0 = A_01_4 + A_01_7;
2707                                    const register double tmp39_0 = A_02_1 + A_02_3 + A_02_4 + A_02_6;
2708                                    const register double tmp123_0 = A_21_2 + A_21_3 + A_21_4 + A_21_5;
2709                                    const register double tmp40_0 = A_02_5 + A_02_7;
2710                                    const register double tmp110_0 = A_02_0 + A_02_7;
2711                                    const register double tmp77_0 = A_12_2 + A_12_3 + A_21_2 + A_21_3;
2712                                    const register double tmp209_0 = A_12_7 + A_21_1;
2713                                    const register double tmp219_0 = A_02_4 + A_20_1;
2714                                    const register double tmp84_0 = A_01_1 + A_01_5 + A_10_2 + A_10_6;
2715                                    const register double tmp162_0 = A_12_1 + A_12_7 + A_21_1 + A_21_7;
2716                                    const register double tmp159_0 = A_01_3 + A_10_3;
2717                                    const register double tmp56_0 = A_11_1 + A_11_3;
2718                                    const register double tmp52_0 = A_01_2 + A_01_5;
2719                                    const register double tmp26_0 = A_00_4 + A_00_5 + A_00_6 + A_00_7;
2720                                    const register double tmp229_0 = A_12_0 + A_12_7 + A_21_1 + A_21_6;
2721                                    const register double tmp151_0 = A_10_2 + A_10_5;
2722                                    const register double tmp136_0 = A_02_0 + A_02_5 + A_20_0 + A_20_5;
2723                                    const register double tmp128_0 = A_21_6 + A_21_7;
2724                                    const register double tmp15_0 = A_12_2 + A_12_4;
2725                                    const register double tmp296_1 = tmp159_0*w42;
2726                                    const register double tmp130_1 = tmp67_0*w5;
2727                                    const register double tmp98_1 = A_01_6*w42;
2728                                    const register double tmp231_1 = tmp125_0*w6;
2729                                    const register double tmp42_1 = tmp34_0*w12;
2730                                    const register double tmp199_1 = A_02_5*w28;
2731                                    const register double tmp113_1 = tmp29_0*w13;
2732                                    const register double tmp330_1 = tmp152_0*w28;
2733                                    const register double tmp90_1 = A_01_1*w46;
2734                                    const register double tmp446_1 = tmp77_0*w22;
2735                                    const register double tmp108_1 = tmp43_0*w5;
2736                                    const register double tmp524_1 = A_12_6*w29;
2737                                    const register double tmp232_1 = tmp126_0*w34;
2738                                    const register double tmp33_1 = tmp25_0*w37;
2739                                    const register double tmp461_1 = tmp180_0*w1;
2740                                    const register double tmp14_1 = tmp8_0*w6;
2741                                    const register double tmp447_1 = tmp205_0*w26;
2742                                    const register double tmp452_1 = tmp198_0*w42;
2743                                    const register double tmp217_1 = tmp81_0*w9;
2744                                    const register double tmp76_1 = tmp59_0*w20;
2745                                    const register double tmp421_1 = tmp134_0*w31;
2746                                    const register double tmp485_1 = tmp51_0*w51;
2747                                    const register double tmp240_1 = tmp131_0*w1;
2748                                    const register double tmp160_1 = tmp91_0*w9;
2749                                    const register double tmp174_1 = A_20_1*w26;
2750                                    const register double tmp273_1 = A_10_1*w46;
2751                                    const register double tmp159_1 = tmp90_0*w47;
2752                                    const register double tmp228_1 = tmp103_0*w5;
2753                                    const register double tmp313_1 = tmp166_0*w45;
2754                                    const register double tmp45_1 = tmp37_0*w30;
2755                                    const register double tmp512_1 = tmp147_0*w13;
2756                                    const register double tmp73_1 = tmp56_0*w43;
2757                                    const register double tmp61_1 = A_01_6*w46;
2758                                    const register double tmp316_1 = tmp167_0*w43;
2759                                    const register double tmp189_1 = tmp112_0*w20;
2760                                    const register double tmp455_1 = tmp215_0*w39;
2761                                    const register double tmp360_1 = A_21_5*w24;
2762                                    const register double tmp258_1 = A_20_7*w2;
2763                                    const register double tmp196_1 = A_20_6*w26;
2764                                    const register double tmp37_1 = tmp29_0*w6;
2765                                    const register double tmp9_1 = A_12_7*w29;
2766                                    const register double tmp80_1 = tmp63_0*w19;
2767                                    const register double tmp312_1 = tmp165_0*w8;
2768                                    const register double tmp264_1 = tmp101_0*w1;
2769                                    const register double tmp124_1 = A_02_3*w26;
2770                                    const register double tmp229_1 = tmp123_0*w11;
2771                                    const register double tmp333_1 = tmp159_0*w46;
2772                                    const register double tmp533_1 = tmp222_0*w4;
2773                                    const register double tmp201_1 = tmp108_0*w37;
2774                                    const register double tmp444_1 = tmp35_0*w10;
2775                                    const register double tmp51_1 = tmp43_0*w18;
2776                                    const register double tmp214_1 = A_21_7*w29;
2777                                    const register double tmp518_1 = tmp86_0*w37;
2778                                    const register double tmp192_1 = tmp115_0*w5;
2779                                    const register double tmp355_1 = A_21_2*w27;
2780                                    const register double tmp156_1 = tmp87_0*w22;
2781                                    const register double tmp516_1 = tmp230_0*w27;
2782                                    const register double tmp366_1 = tmp104_0*w57;
2783                                    const register double tmp271_1 = tmp146_0*w49;
2784                                    const register double tmp437_1 = tmp218_0*w24;
2785                                    const register double tmp436_1 = tmp104_0*w54;
2786                                    const register double tmp167_1 = tmp98_0*w8;
2787                                    const register double tmp136_1 = tmp70_0*w34;
2788                                    const register double tmp406_1 = tmp207_0*w27;
2789                                    const register double tmp193_1 = tmp116_0*w12;
2790                                    const register double tmp486_1 = tmp225_0*w29;
2791                                    const register double tmp469_1 = tmp224_0*w11;
2792                                    const register double tmp287_1 = tmp71_0*w53;
2793                                    const register double tmp430_1 = tmp213_0*w28;
2794                                    const register double tmp462_1 = tmp220_0*w2;
2795                                    const register double tmp294_1 = tmp53_0*w59;
2796                                    const register double tmp218_1 = tmp118_0*w16;
2797                                    const register double tmp116_1 = tmp25_0*w31;
2798                                    const register double tmp495_1 = tmp76_0*w37;
2799                                    const register double tmp501_1 = tmp99_0*w46;
2800                                    const register double tmp0_1 = tmp0_0*w1;
2801                                    const register double tmp99_1 = tmp62_0*w17;
2802                                    const register double tmp429_1 = tmp212_0*w2;
2803                                    const register double tmp249_1 = tmp136_0*w9;
2804                                    const register double tmp504_1 = tmp229_0*w19;
2805                                    const register double tmp197_1 = A_12_2*w27;
2806                                    const register double tmp531_1 = tmp122_0*w35;
2807                                    const register double tmp265_1 = tmp142_0*w46;
2808                                    const register double tmp488_1 = tmp226_0*w4;
2809                                    const register double tmp528_1 = tmp115_0*w18;
2810                                    const register double tmp438_1 = tmp219_0*w2;
2811                                    const register double tmp233_1 = tmp127_0*w13;
2812                                    const register double tmp491_1 = tmp79_0*w1;
2813                                    const register double tmp215_1 = A_21_0*w4;
2814                                    const register double tmp24_1 = tmp18_0*w21;
2815                                    const register double tmp538_1 = tmp209_0*w27;
2816                                    const register double tmp379_1 = tmp167_0*w55;
2817                                    const register double tmp332_1 = tmp154_0*w4;
2818                                    const register double tmp498_1 = tmp68_0*w31;
2819                                    const register double tmp41_1 = tmp33_0*w33;
2820                                    const register double tmp464_1 = tmp179_0*w37;
2821                                    const register double tmp317_1 = tmp168_0*w40;
2822                                    const register double tmp378_1 = tmp106_0*w54;
2823                                    const register double tmp184_1 = tmp109_0*w14;
2824                                    const register double tmp292_1 = tmp14_0*w33;
2825                                    const register double tmp11_1 = tmp5_0*w11;
2826                                    const register double tmp354_1 = A_02_6*w26;
2827                                    const register double tmp84_1 = tmp37_0*w0;
2828                                    const register double tmp422_1 = tmp13_0*w30;
2829                                    const register double tmp132_1 = tmp69_0*w11;
2830                                    const register double tmp251_1 = tmp138_0*w31;
2831                                    const register double tmp18_1 = tmp12_0*w8;
2832                                    const register double tmp88_1 = A_21_1*w4;
2833                                    const register double tmp188_1 = A_12_2*w24;
2834                                    const register double tmp465_1 = tmp175_0*w31;
2835                                    const register double tmp235_1 = tmp128_0*w17;
2836                                    const register double tmp323_1 = A_02_1*w26;
2837                                    const register double tmp31_1 = tmp23_0*w38;
2838                                    const register double tmp397_1 = tmp170_0*w5;
2839                                    const register double tmp175_1 = tmp7_0*w3;
2840                                    const register double tmp148_1 = tmp81_0*w21;
2841                                    const register double tmp238_1 = tmp130_0*w19;
2842                                    const register double tmp59_1 = tmp46_0*w11;
2843                                    const register double tmp432_1 = tmp215_0*w35;
2844                                    const register double tmp398_1 = A_01_2*w46;
2845                                    const register double tmp497_1 = A_10_5*w46;
2846                                    const register double tmp28_1 = tmp21_0*w18;
2847                                    const register double tmp115_1 = tmp23_0*w32;
2848                                    const register double tmp441_1 = tmp23_0*w3;
2849                                    const register double tmp131_1 = tmp68_0*w37;
2850                                    const register double tmp289_1 = tmp155_0*w4;
2851                                    const register double tmp278_1 = tmp80_0*w44;
2852                                    const register double tmp5_1 = A_21_4*w27;
2853                                    const register double tmp254_1 = tmp140_0*w20;
2854                                    const register double tmp183_1 = tmp108_0*w31;
2855                                    const register double tmp279_1 = tmp151_0*w8;
2856                                    const register double tmp298_1 = tmp161_0*w16;
2857                                    const register double tmp505_1 = tmp230_0*w24;
2858                                    const register double tmp246_1 = tmp80_0*w52;
2859                                    const register double tmp100_1 = tmp53_0*w43;
2860                                    const register double tmp440_1 = tmp221_0*w16;
2861                                    const register double tmp481_1 = tmp188_0*w23;
2862                                    const register double tmp480_1 = tmp187_0*w35;
2863                                    const register double tmp384_1 = tmp150_0*w53;
2864                                    const register double tmp142_1 = tmp76_0*w31;
2865                                    const register double tmp372_1 = tmp191_0*w11;
2866                                    const register double tmp307_1 = A_10_7*w35;
2867                                    const register double tmp186_1 = tmp111_0*w19;
2868                                    const register double tmp127_1 = A_20_2*w2;
2869                                    const register double tmp391_1 = tmp167_0*w59;
2870                                    const register double tmp223_1 = tmp113_0*w20;
2871                                    const register double tmp454_1 = tmp197_0*w24;
2872                                    const register double tmp241_1 = tmp74_0*w51;
2873                                    const register double tmp529_1 = tmp114_0*w5;
2874                                    const register double tmp202_1 = tmp104_0*w7;
2875                                    const register double tmp236_1 = tmp96_0*w21;
2876                                    const register double tmp358_1 = tmp183_0*w11;
2877                                    const register double tmp102_1 = tmp51_0*w41;
2878                                    const register double tmp493_1 = A_20_5*w2;
2879                                    const register double tmp468_1 = tmp223_0*w4;
2880                                    const register double tmp435_1 = tmp217_0*w16;
2881                                    const register double tmp110_1 = tmp37_0*w36;
2882                                    const register double tmp479_1 = tmp189_0*w4;
2883                                    const register double tmp120_1 = tmp38_0*w22;
2884                                    const register double tmp16_1 = tmp10_0*w9;
2885                                    const register double tmp407_1 = tmp90_0*w53;
2886                                    const register double tmp442_1 = tmp66_0*w48;
2887                                    const register double tmp60_1 = A_10_4*w35;
2888                                    const register double tmp69_1 = tmp53_0*w45;
2889                                    const register double tmp144_1 = tmp77_0*w17;
2890                                    const register double tmp507_1 = tmp146_0*w48;
2891                                    const register double tmp424_1 = tmp174_0*w18;
2892                                    const register double tmp352_1 = tmp181_0*w23;
2893                                    const register double tmp451_1 = tmp199_0*w13;
2894                                    const register double tmp253_1 = tmp139_0*w16;
2895                                    const register double tmp353_1 = tmp182_0*w18;
2896                                    const register double tmp521_1 = tmp88_0*w22;
2897                                    const register double tmp346_1 = tmp175_0*w37;
2898                                    const register double tmp416_1 = tmp138_0*w37;
2899                                    const register double tmp324_1 = A_10_0*w35;
2900                                    const register double tmp152_1 = tmp84_0*w37;
2901                                    const register double tmp119_1 = tmp32_0*w21;
2902                                    const register double tmp86_1 = A_21_6*w29;
2903                                    const register double tmp290_1 = tmp156_0*w11;
2904                                    const register double tmp382_1 = tmp196_0*w26;
2905                                    const register double tmp91_1 = tmp49_0*w6;
2906                                    const register double tmp499_1 = A_10_2*w42;
2907                                    const register double tmp226_1 = tmp121_0*w13;
2908                                    const register double tmp477_1 = tmp195_0*w26;
2909                                    const register double tmp150_1 = A_02_4*w23;
2910                                    const register double tmp318_1 = tmp15_0*w22;
2911                                    const register double tmp396_1 = tmp206_0*w24;
2912                                    const register double tmp474_1 = A_02_0*w28;
2913                                    const register double tmp245_1 = tmp134_0*w37;
2914                                    const register double tmp3_1 = A_20_4*w26;
2915                                    const register double tmp44_1 = tmp36_0*w31;
2916                                    const register double tmp487_1 = tmp60_0*w52;
2917                                    const register double tmp293_1 = tmp158_0*w8;
2918                                    const register double tmp314_1 = A_01_2*w42;
2919                                    const register double tmp414_1 = tmp80_0*w51;
2920                                    const register double tmp472_1 = A_21_3*w27;
2921                                    const register double tmp321_1 = A_21_2*w24;
2922                                    const register double tmp225_1 = tmp120_0*w6;
2923                                    const register double tmp377_1 = tmp166_0*w59;
2924                                    const register double tmp413_1 = tmp186_0*w26;
2925                                    const register double tmp385_1 = tmp166_0*w55;
2926                                    const register double tmp310_1 = tmp164_0*w34;
2927                                    const register double tmp158_1 = tmp89_0*w34;
2928                                    const register double tmp449_1 = tmp203_0*w46;
2929                                    const register double tmp439_1 = tmp220_0*w28;
2930                                    const register double tmp22_1 = tmp16_0*w16;
2931                                    const register double tmp164_1 = tmp95_0*w46;
2932                                    const register double tmp417_1 = tmp74_0*w52;
2933                                    const register double tmp257_1 = tmp6_0*w25;
2934                                    const register double tmp203_1 = tmp18_0*w9;
2935                                    const register double tmp286_1 = tmp153_0*w28;
2936                                    const register double tmp155_1 = tmp33_0*w14;
2937                                    const register double tmp389_1 = tmp201_0*w12;
2938                                    const register double tmp508_1 = tmp145_0*w49;
2939                                    const register double tmp300_1 = tmp56_0*w55;
2940                                    const register double tmp299_1 = tmp162_0*w22;
2941                                    const register double tmp173_1 = tmp104_0*w25;
2942                                    const register double tmp32_1 = tmp24_0*w5;
2943                                    const register double tmp227_1 = tmp122_0*w39;
2944                                    const register double tmp484_1 = tmp3_0*w38;
2945                                    const register double tmp171_1 = tmp102_0*w21;
2946                                    const register double tmp478_1 = tmp190_0*w29;
2947                                    const register double tmp320_1 = tmp170_0*w18;
2948                                    const register double tmp327_1 = tmp6_0*w57;
2949                                    const register double tmp490_1 = tmp7_0*w32;
2950                                    const register double tmp419_1 = tmp127_0*w6;
2951                                    const register double tmp463_1 = tmp219_0*w28;
2952                                    const register double tmp12_1 = tmp6_0*w7;
2953                                    const register double tmp49_1 = tmp41_0*w22;
2954                                    const register double tmp344_1 = tmp173_0*w26;
2955                                    const register double tmp243_1 = tmp132_0*w2;
2956                                    const register double tmp83_1 = A_10_4*w39;
2957                                    const register double tmp297_1 = tmp160_0*w17;
2958                                    const register double tmp275_1 = tmp148_0*w34;
2959                                    const register double tmp168_1 = tmp99_0*w42;
2960                                    const register double tmp409_1 = tmp3_0*w32;
2961                                    const register double tmp1_1 = tmp1_0*w25;
2962                                    const register double tmp426_1 = tmp210_0*w39;
2963                                    const register double tmp375_1 = tmp109_0*w33;
2964                                    const register double tmp50_1 = tmp42_0*w19;
2965                                    const register double tmp513_1 = A_10_1*w42;
2966                                    const register double tmp97_1 = tmp45_0*w31;
2967                                    const register double tmp403_1 = tmp140_0*w1;
2968                                    const register double tmp71_1 = A_01_1*w42;
2969                                    const register double tmp520_1 = tmp84_0*w31;
2970                                    const register double tmp510_1 = A_10_6*w46;
2971                                    const register double tmp302_1 = A_10_0*w39;
2972