util_quda.h File Reference

#include <stdio.h>
#include <stdlib.h>
#include <enum_quda.h>
#include <comm_quda.h>
#include <tune_key.h>

Include dependency graph for util_quda.h:

This graph shows which files directly or indirectly include this file:

Go to the source code of this file.

Macros
#define	zeroThread
#define	printfZero(...)
#define	printfQuda(...)
#define	errorQuda(...)
#define	warningQuda(...)
#define	checkCudaErrorNoSync()
#define	checkCudaError()   checkCudaErrorNoSync()

Functions
QudaTune	getTuning ()
	Query whether autotuning is enabled or not. Default is enabled but can be overridden by setting QUDA_ENABLE_TUNING=0. More...
QudaVerbosity	getVerbosity ()
char *	getOutputPrefix ()
FILE *	getOutputFile ()
void	setVerbosity (const QudaVerbosity verbosity)
void	setOutputPrefix (const char *prefix)
void	setOutputFile (FILE *outfile)
void	pushVerbosity (QudaVerbosity verbosity)
void	popVerbosity ()
bool	getRankVerbosity ()
	This function returns true if the calling rank is enabled for verbosity (e.g., whether printQuda and warningQuda will print out from this rank). More...
char *	getPrintBuffer ()

Macro Definition Documentation

checkCudaError

#define checkCudaError

(

)

checkCudaErrorNoSync()

Definition at line 129 of file util_quda.h.

Referenced by quda::ApplyClover(), quda::ApplyTwistClover(), quda::ApplyTwistGamma(), quda::applyU(), quda::cudaGaugeField::backup(), Spinor< RegType, StoreType, N, write, tex_id >::backup(), quda::cudaColorSpinorField::backup(), blasCuda(), quda::calculateY(), comm_declare_receive_relative_(), comm_declare_send_relative_(), comm_declare_strided_receive_relative_(), comm_declare_strided_send_relative_(), quda::computeCloverForce(), computeCloverForceQuda(), quda::computeCloverSigmaOprod(), computeGaugeFixingFFTQuda(), computeGaugeFixingOVRQuda(), computeGaugeForceQuda(), computeStaggeredForceQuda(), quda::contractCuda(), quda::blas::copy_ns::copy(), quda::cudaCloverField::copy(), quda::cudaGaugeField::copy(), quda::cpuGaugeField::copy(), quda::copyGaugeEx(), quda::copySpinorEx(), quda::LatticeField::createComms(), quda::createDslashEvents(), quda::Transfer::createGeoMap(), quda::LatticeField::createIPCComms(), quda::LatticeField::destroyComms(), quda::destroyDslashEvents(), quda::LatticeField::destroyIPCComms(), quda::extractGhostEx(), quda::fatLongKSLink(), hisq_force_test(), init(), initFields(), initQudaMemory(), quda::blas::initReduce(), quda::clover::FloatNOrder< Float, length, N, huge_alloc >::load(), quda::colorspinor::FloatNOrder< Float, Ns, Nc, N, huge_alloc >::load(), quda::gauge::FloatNOrder< Float, length, N, reconLenParam, stag_phase, huge_alloc >::load(), loadCloverQuda(), quda::cudaGaugeField::loadCPUField(), momActionQuda(), multiblasCuda(), multiReduceCuda(), quda::projectSU3(), quda::Prolongate(), quda::qudaMemcpy_(), reduceCuda(), register_pinned_quda_(), quda::GMResDR::RestartVZH(), quda::cudaGaugeField::restore(), Spinor< RegType, StoreType, N, write, tex_id >::restore(), quda::cudaColorSpinorField::restore(), quda::clover::FloatNOrder< Float, length, N, huge_alloc >::save(), quda::colorspinor::FloatNOrder< Float, Ns, Nc, N, huge_alloc >::save(), quda::gauge::FloatNOrder< Float, length, N, reconLenParam, stag_phase, huge_alloc >::save(), quda::cudaGaugeField::saveCPUField(), unregister_pinned_quda_(), updateGaugeFieldQuda(), quda::updateMomentum(), and quda::cudaCloverField::~cudaCloverField().

checkCudaErrorNoSync

#define checkCudaErrorNoSync

(

)

Value:

do {                    \
  cudaError_t error = cudaGetLastError();              \
  if (error != cudaSuccess)                            \
    errorQuda("(CUDA) %s", cudaGetErrorString(error)); \
} while (0)

Definition at line 113 of file util_quda.h.

Referenced by comm_peer2peer_init(), and initQudaDevice().

errorQuda

#define errorQuda

(

...

)

Value:

do {                 \
  fprintf(getOutputFile(), "%sERROR: ", getOutputPrefix());        \
  fprintf(getOutputFile(), __VA_ARGS__);             \
  fprintf(getOutputFile(), " (" __FILE__ ":%d in %s())\n",         \
    __LINE__, __func__);                 \
  fprintf(getOutputFile(), "%s       last kernel called was (name=%s,volume=%s,aux=%s)\n", \
    getOutputPrefix(), getLastTuneKey().name,          \
    getLastTuneKey().volume, getLastTuneKey().aux);        \
  comm_abort(1);                     \
} while (0)

Definition at line 90 of file util_quda.h.

Referenced by quda::gauge::Accessor< Float, nColor, order >::Accessor(), quda::clover::Accessor< Float, nColor, nSpin, order >::Accessor(), quda::colorspinor::AccessorCB< Float, nSpin, nColor, nVec, order >::AccessorCB(), quda::Tunable::advanceBlockDim(), quda::ShiftColorSpinorField< Output, Input >::advanceBlockDim(), MultiReduceCuda< NXZ, doubleN, ReduceType, FloatN, M, SpinorX, SpinorY, SpinorZ, SpinorW, Reducer >::advanceGridDim(), quda::aligned_malloc(), quda::RNG::AllocateRNG(), quda::APEStep(), quda::QudaMemCopy::apply(), quda::ShiftColorSpinorField< Output, Input >::apply(), quda::ArpackArgs< Float >::apply(), quda::Gamma< ValueType, basis, dir >::apply(), quda::TwistGamma< Float, nColor, Arg >::apply(), quda::GaugeOvrImpSTOUT< Float, GaugeOr, GaugeDs >::apply(), quda::DslashCoarsePolicyTune::apply(), quda::CalculateY< from_coarse, Float, fineSpin, fineColor, coarseSpin, coarseColor, Arg >::apply(), anonymous_namespace{dslash_policy.cuh}::DslashPolicyTune::apply(), apply_clover(), apply_staggered_phase_quda_(), quda::ApplyClover(), quda::ApplyCovDev(), quda::ApplyGamma(), quda::applyGaugePhase(), quda::GaugeField::applyStaggeredPhase(), applyTwist(), quda::ApplyTwistClover(), quda::applyU(), quda::arpackSolve(), quda::asymCloverDslashCuda(), quda::blas::axCpu(), quda::blas::axpbyCpu(), quda::blas::axpyCpu(), quda::RNG::backup(), quda::cudaGaugeField::backup(), quda::LatticeField::backup(), quda::cpuGaugeField::backup(), quda::cudaColorSpinorField::backup(), quda::cpuColorSpinorField::backup(), quda::cublas::BatchInvertMatrix(), benchmark(), bindSpinorTex(), blasCuda(), mixed::blasCuda(), quda::BlockOrthogonalize(), quda::gauge::BQCDOrder< Float, length >::BQCDOrder(), quda::CalculateY< from_coarse, Float, fineSpin, fineColor, coarseSpin, coarseColor, Arg >::bytes(), quda::calculateY(), quda::CalculateYArg< Float, coarseGauge, fineGauge, fineSpinor, fineSpinorTmp, fineClover >::CalculateYArg(), GaugeAlgTest::CallUnitarizeLinks(), CallUnitarizeLinks(), quda::blas::caxpbyCpu(), quda::blas::caxpbypzYmbwCpu(), quda::blas::caxpy_L(), quda::blas::caxpy_U(), quda::blas::caxpyCpu(), quda::blas::caxpyXmazMR(), quda::blas::cDotProduct(), quda::blas::cDotProductCopy(), quda::blas::cDotProductCpu(), check_displacement(), checkClover(), quda::GaugeField::checkField(), quda::ColorSpinorField::checkField(), quda::LatticeField::checkField(), quda::Dirac::checkFullSpinor(), checkGauge(), quda::Tunable::checkLaunchParam(), checkLength(), quda::checkMomOrder(), quda::checkNan(), quda::Dirac::checkParitySpinor(), quda::DiracClover::checkParitySpinor(), quda::DiracTwistedClover::checkParitySpinor(), quda::DiracStaggered::checkParitySpinor(), quda::DiracImprovedStaggered::checkParitySpinor(), checkSpinor(), quda::Dirac::checkSpinorAlias(), quda::Checksum(), checkTypes(), CloseMagma(), quda::DiracCoarse::Clover(), clover_matpc(), quda::CloverArg< Float, nSpin, nColor, dynamic_clover_ >::CloverArg(), quda::cloverDerivative(), quda::cloverDslashCuda(), quda::DiracCoarse::CloverInv(), quda::cloverInvert(), cloverQuda(), quda::CoarseCoarseOp(), quda::CoarseOp(), quda::ColorSpinorParam::ColorSpinorParam(), quda::colorSpinorParam(), comm_allreduce_xor(), comm_create_topology(), comm_declare_receive_displaced(), comm_declare_receive_relative_(), comm_declare_send_displaced(), comm_declare_send_relative_(), comm_declare_strided_receive_displaced(), comm_declare_strided_receive_relative_(), comm_declare_strided_send_displaced(), comm_declare_strided_send_relative_(), comm_default_topology(), comm_gdr_blacklist(), comm_init(), comm_peer2peer_init(), comm_set_neighbor_ranks(), anonymous_namespace{dslash_policy.cuh}::commsComplete(), quda::LatticeField::commsQuery(), quda::cudaColorSpinorField::commsQuery(), quda::LatticeField::commsStart(), quda::LatticeField::commsWait(), quda::cudaColorSpinorField::commsWait(), quda::completeKSForce(), quda::ColorSpinorField::Component(), quda::cudaColorSpinorField::Component(), quda::CompositeColorSpinorFieldDescriptor::CompositeColorSpinorFieldDescriptor(), quda::cudaCloverField::compute(), compute_gauge_force_quda_(), quda::computeClover(), quda::computeCloverForce(), computeCloverForceQuda(), quda::computeCloverSigmaOprod(), quda::computeCloverSigmaTrace(), quda::ComputeEta(), quda::ComputeEta< libtype::magma_lib >(), quda::computeFmunu(), computeGaugeForceQuda(), quda::ComputeHarmonicRitz(), quda::ComputeHarmonicRitz< libtype::magma_lib >(), computeHISQForceQuda(), computeKSLinkQuda(), quda::computeKSLongLinkForce(), quda::computeMomAction(), quda::computeQCharge(), quda::ComputeRitz(), quda::ComputeRitz< libtype::magma_lib >(), computeStaggeredForceQuda(), quda::computeStaggeredOprod(), contract(), quda::contractCuda(), quda::blas::copy_ns::copy(), quda::copy(), quda::cudaCloverField::copy(), quda::cudaGaugeField::copy(), quda::cpuGaugeField::copy(), quda::cudaColorSpinorField::copy(), quda::CopyColorSpinor< FloatOut, FloatIn, Ns, Nc, Arg >::CopyColorSpinor(), quda::CopyColorSpinor< FloatOut, FloatIn, 4, Nc, Arg >::CopyColorSpinor(), quda::copyExtendedColorSpinor(), quda::CopyExtendedColorSpinor(), quda::copyExtendedGauge(), quda::CopyGauge< FloatOut, FloatIn, length, OutOrder, InOrder, isGhost >::CopyGauge(), quda::copyGauge(), quda::copyGaugeEx(), quda::copyGaugeMG(), quda::copyGenericClover(), quda::CopyGenericColorSpinor(), quda::copyGenericColorSpinor(), quda::copyGenericColorSpinorMGDD(), quda::copyGenericColorSpinorMGDS(), quda::copyGenericColorSpinorMGSD(), quda::copyGenericColorSpinorMGSS(), quda::copyGenericGauge(), quda::copyGenericGaugeDoubleOut(), quda::copyGenericGaugeHalfOut(), quda::copyGenericGaugeMG(), quda::copyGenericGaugeSingleOut(), quda::copyMom(), quda::copySpinorEx(), quda::cudaColorSpinorField::copySpinorField(), quda::cudaColorSpinorField::CopySubset(), quda::gauge::CPSOrder< Float, length >::CPSOrder(), quda::cpuCloverField::cpuCloverField(), quda::cpuColorSpinorField::cpuColorSpinorField(), quda::cpuGaugeField::cpuGaugeField(), quda::Eig_Solver::create(), quda::Dirac::create(), quda::ColorSpinorField::create(), quda::Solver::create(), quda::ColorSpinorField::Create(), quda::cudaColorSpinorField::create(), quda::cpuColorSpinorField::create(), anonymous_namespace{dslash_policy.cuh}::DslashFactory::create(), createCloverQuda(), quda::ColorSpinorField::CreateCoarse(), quda::Dirac::createCoarseOp(), quda::ColorSpinorField::CreateFine(), createGaugeFieldQuda(), quda::ColorSpinorField::createGhostZone(), quda::LatticeField::createIPCComms(), quda::cudaCloverField::cudaCloverField(), quda::cudaGaugeField::cudaGaugeField(), quda::blas::cxpaypbzCpu(), quda::DeflationParam::DeflationParam(), quda::deserializeTuneCache(), quda::cudaColorSpinorField::destroy(), quda::device_free_(), quda::pool::device_free_(), quda::device_malloc_(), quda::gauge::Accessor< Float, nColor, QUDA_QDP_GAUGE_ORDER >::device_norm2(), quda::gauge::Accessor< Float, nColor, QUDA_MILC_GAUGE_ORDER >::device_norm2(), quda::gauge::Accessor< Float, nColor, QUDA_FLOAT2_GAUGE_ORDER >::device_norm2(), quda::device_pinned_free_(), quda::device_pinned_malloc_(), quda::DiracCloverPC::DiracCloverPC(), quda::domainWallDslashCuda(), quda::DiracWilson::Dslash(), quda::DiracCloverPC::Dslash(), quda::DiracDomainWall::Dslash(), quda::DiracTwistedMassPC::Dslash(), quda::DiracTwistedCloverPC::Dslash(), quda::DiracStaggered::Dslash(), quda::DiracImprovedStaggered::Dslash(), quda::DiracCoarse::Dslash(), quda::DiracCoarsePC::Dslash(), quda::DiracDomainWall4DPC::Dslash4(), quda::DiracMobius::Dslash4(), quda::DiracMobius::Dslash4pre(), quda::DiracMobius::Dslash4preXpay(), quda::DiracDomainWall4DPC::Dslash4Xpay(), quda::DiracMobius::Dslash4Xpay(), quda::DiracDomainWall4DPC::Dslash5(), quda::DiracMobius::Dslash5(), quda::DiracDomainWall4DPC::Dslash5inv(), quda::DiracMobiusPC::Dslash5inv(), quda::DiracDomainWall4DPC::Dslash5invXpay(), quda::DiracMobiusPC::Dslash5invXpay(), quda::DiracDomainWall4DPC::Dslash5Xpay(), quda::DiracMobius::Dslash5Xpay(), dslash_4_4d(), quda::DslashCoarsePolicyTune::DslashCoarsePolicyTune(), dslashCUDA(), DslashCuda::DslashCuda(), anonymous_namespace{dslash_policy.cuh}::DslashPolicyTune::DslashPolicyTune(), dslashQuda(), dslashQuda_4dpc(), dslashQuda_mdwf(), dslashRef(), quda::DiracWilson::DslashXpay(), quda::DiracClover::DslashXpay(), quda::DiracCloverPC::DslashXpay(), quda::DiracDomainWall::DslashXpay(), quda::DiracTwistedMassPC::DslashXpay(), quda::DiracTwistedCloverPC::DslashXpay(), quda::DiracStaggered::DslashXpay(), quda::DiracImprovedStaggered::DslashXpay(), quda::DiracCoarse::DslashXpay(), dw_dslash(), quda::IncEigCG::eigCGsolve(), quda::ColorSpinorField::Even(), quda::GaugeField::Even_p(), quda::GaugeField::exchange(), quda::cudaGaugeField::exchangeGhost(), quda::cpuGaugeField::exchangeGhost(), quda::cudaColorSpinorField::exchangeGhost(), quda::extendedCopyColorSpinor(), quda::extractExtendedGaugeGhost(), quda::extractGaugeGhost(), quda::extractGaugeGhostMG(), quda::extractGhost(), quda::extractGhostEx(), quda::extractGhostMG(), quda::fatLongKSLink(), quda::gauge::FieldOrder< Float, nColor, nSpinCoarse, order, native_ghost >::FieldOrder(), quda::FillV(), quda::clover::FloatNOrder< Float, length, N, huge_alloc >::FloatNOrder(), quda::colorspinor::FloatNOrder< Float, Ns, Nc, N, huge_alloc >::FloatNOrder(), quda::gauge::FloatNOrder< Float, length, N, reconLenParam, stag_phase, huge_alloc >::FloatNOrder(), quda::CalculateY< from_coarse, Float, fineSpin, fineColor, coarseSpin, coarseColor, Arg >::flops(), flushChronoQuda(), freeCloverQuda(), freeGaugeQuda(), freeSloppyCloverQuda(), freeSloppyGaugeQuda(), quda::GammaArg< Float, nColor >::GammaArg(), quda::LatticeField::gather(), gauge_force_test(), quda::GaugeField::Gauge_p(), quda::GaugeField::GaugeField(), quda::GaugeFieldParam::GaugeFieldParam(), quda::gaugefixingFFT(), quda::gaugefixingOVR(), quda::gaugeForce(), quda::gaugeGauss(), gaussGaugeQuda(), quda::gaussSpinor(), quda::GCR::GCR(), quda::MG::generateNullVectors(), genericBlas(), quda::genericCompare(), quda::genericCopyColorSpinor(), genericMultiBlas(), quda::genericPrintVector(), genericReduce(), quda::genericSource(), get_prec(), get_solver_str(), get_su3_matrix(), quda::getLinkDeterminant(), quda::getLinkTrace(), Locator< oddBit >::getNeighborFromFullIndex(), quda::Dirac::getStencilSteps(), quda::GaugeField::Ghost(), quda::ColorSpinorField::Ghost(), quda::gauge::GhostAccessor< Float, nColor, order, native_ghost >::GhostAccessor(), quda::colorspinor::GhostAccessorCB< Float, nSpin, nColor, nVec, order >::GhostAccessorCB(), quda::ColorSpinorField::GhostNorm(), quda::GMResDR::GMResDR(), quda::blas::hDotProduct(), quda::blas::hDotProduct_Anorm(), quda::blas::HeavyQuarkResidualNormCpu(), hisq_force_init(), hisq_force_test(), hisqCompleteForceCPU(), hisqLongLinkForceCPU(), hisqStaplesForceCPU(), quda::host_free_(), quda::improvedStaggeredDslashCuda(), quda::IncEigCG::IncEigCG(), quda::Deflation::increment(), init(), init_default_comms(), initComms(), initCommsGridQuda(), initFields(), quda::InitGaugeField(), initQudaDevice(), quda::ShiftColorSpinorField< Output, Input >::initTuneParam(), quda::Tunable::initTuneParam(), quda::cudaGaugeField::injectGhost(), quda::cpuGaugeField::injectGhost(), invert_multishift_quda_(), invert_test(), invertMultiShiftQuda(), invertMultiSrcQuda(), invertQuda(), anonymous_namespace{dslash_policy.cuh}::issuePack(), lanczosQuda(), quda::LatticeFieldParam::LatticeFieldParam(), quda::gauge::LegacyOrder< Float, length >::LegacyOrder(), loadCloverQuda(), loadGaugeQuda(), loadSloppyGaugeQuda(), quda::loadTuneCache(), quda::Deflation::loadVectors(), quda::MG::loadVectors(), quda::LatticeField::Location(), quda::Location_(), quda::DiracWilsonPC::M(), quda::DiracDomainWallPC::M(), quda::DiracDomainWall4DPC::M(), quda::DiracMobius::M(), quda::DiracMobiusPC::M(), quda::DiracTwistedMass::M(), quda::DiracTwistedClover::M(), quda::DiracTwistedCloverPC::M(), quda::DiracStaggeredPC::M(), quda::DiracImprovedStaggeredPC::M(), quda::DiracCoarse::M(), quda::DiracCoarsePC::M(), quda::GaugeLaplacePC::M(), magma_Xgeev(), magma_Xgels(), magma_Xgesv(), magma_Xheev(), main(), quda::mapped_malloc_(), quda::massRescale(), MatDagMatQuda(), MatQuda(), quda::Tunable::maxBlocksPerSM(), quda::maxGauge(), quda::DiracStaggeredPC::MdagM(), quda::DiracImprovedStaggeredPC::MdagM(), quda::DiracCoarse::MdagM(), mdw_matpc(), quda::MDWFDslashCuda(), quda::MG::MG(), quda::CalculateY< from_coarse, Float, fineSpin, fineColor, coarseSpin, coarseColor, Arg >::minThreads(), momActionQuda(), quda::Monte(), mixed::multiblasCuda(), multiblasCuda(), quda::multigrid_solver::multigrid_solver(), mixed::multiReduceCuda(), multiReduceCuda(), multiReduceLaunch(), quda::blas::mxpyCpu(), quda::ndegTwistedMassDslashCuda(), quda::blas::norm1(), quda::blas::normCpu(), quda::LatticeField::Nvec(), quda::ColorSpinorField::Odd(), quda::GaugeField::Odd_p(), OpenMagma(), quda::Deflation::operator()(), quda::MG::operator()(), quda::CG::operator()(), quda::MPCG::operator()(), anonymous_namespace{dslash_policy.cuh}::DslashPthreads::operator()(), quda::BiCGstab::operator()(), quda::MPBiCGstab::operator()(), quda::BiCGstabL::operator()(), quda::GCR::operator()(), quda::MultiShiftCG::operator()(), quda::IncEigCG::operator()(), quda::DslashCoarseLaunch::operator()(), anonymous_namespace{dslash_policy.cuh}::DslashAsync::operator()(), anonymous_namespace{dslash_policy.cuh}::DslashFusedExteriorAsync::operator()(), quda::Dirac::operator=(), quda::cudaColorSpinorField::operator=(), quda::cpuColorSpinorField::operator=(), quda::orthoDir(), quda::BiCGstabL::orthoDir(), quda::OvrImpSTOUTStep(), quda::Transfer::P(), quda::cudaColorSpinorField::packGhost(), quda::cudaColorSpinorField::packGhostExtended(), performAPEnStep(), performOvrImpSTOUTnStep(), performSTOUTnStep(), performWuppertalnStep(), quda::PGaugeExchange(), quda::pool::pinned_free_(), quda::pinned_malloc_(), plaqQuda(), quda::plaquette(), popVerbosity(), quda::CalculateY< from_coarse, Float, fineSpin, fineColor, coarseSpin, coarseColor, Arg >::postTune(), SpinorTexture< RegType, StoreType, N, tex_id >::Precision(), quda::Precision_(), quda::PreconCG::PreconCG(), quda::DiracWilson::prepare(), quda::DiracWilsonPC::prepare(), quda::DiracClover::prepare(), quda::DiracCloverPC::prepare(), quda::DiracDomainWall::prepare(), quda::DiracDomainWallPC::prepare(), quda::DiracDomainWall4DPC::prepare(), quda::DiracMobius::prepare(), quda::DiracMobiusPC::prepare(), quda::DiracTwistedMass::prepare(), quda::DiracTwistedMassPC::prepare(), quda::DiracTwistedClover::prepare(), quda::DiracTwistedCloverPC::prepare(), quda::DiracStaggered::prepare(), quda::DiracImprovedStaggered::prepare(), quda::DiracCoarse::prepare(), quda::DiracCoarsePC::prepare(), quda::GaugeLaplace::prepare(), quda::GaugeLaplacePC::prepare(), quda::CalculateY< from_coarse, Float, fineSpin, fineColor, coarseSpin, coarseColor, Arg >::preTune(), printQudaMultigridParam(), quda::Solver::PrintStats(), quda::projectSU3(), projectSU3Quda(), quda::Prolongate(), quda::colorspinor::QDPJITDiracOrder< Float, Ns, Nc >::QDPJITDiracOrder(), quda::qudaDeviceSynchronize(), quda::qudaEventQuery(), quda::qudaEventRecord(), quda::qudaEventSynchronize(), quda::qudaLaunchKernel(), quda::QudaMemCopy::QudaMemCopy(), quda::qudaMemcpy2DAsync_(), quda::qudaMemcpyAsync_(), quda::qudaStreamSynchronize(), quda::qudaStreamWaitEvent(), quda::Transfer::R(), quda::LatticeField::read(), read_field(), read_gauge_field(), read_spinor_field(), quda::DiracWilsonPC::reconstruct(), quda::DiracCloverPC::reconstruct(), quda::DiracDomainWallPC::reconstruct(), quda::DiracDomainWall4DPC::reconstruct(), quda::DiracMobiusPC::reconstruct(), quda::DiracTwistedMassPC::reconstruct(), quda::DiracTwistedCloverPC::reconstruct(), quda::DiracCoarsePC::reconstruct(), quda::GaugeLaplacePC::reconstruct(), quda::cudaColorSpinorField::recvStart(), quda::blas::reDotProduct(), quda::blas::reDotProductCpu(), quda::Deflation::reduce(), reduceCuda(), mixed::reduceCuda(), reduceLaunch(), remove_staggered_phase_quda_(), quda::GaugeField::removeStaggeredPhase(), quda::Timer::Reset(), quda::ColorSpinorField::reset(), quda::IncEigCG::RestartVT(), quda::GMResDR::RestartVZH(), quda::RNG::restore(), quda::cudaGaugeField::restore(), quda::LatticeField::restore(), quda::cpuGaugeField::restore(), quda::cudaColorSpinorField::restore(), quda::cpuColorSpinorField::restore(), quda::Restrict(), quda::safe_malloc_(), quda::ArpackArgs< Float >::save(), quda::clover::FloatNOrder< Float, length, N, huge_alloc >::save(), quda::colorspinor::FloatNOrder< Float, Ns, Nc, N, huge_alloc >::save(), quda::gauge::FloatNOrder< Float, length, N, reconLenParam, stag_phase, huge_alloc >::save(), quda::cudaCloverField::saveCPUField(), quda::cudaGaugeField::saveCPUField(), saveGaugeQuda(), quda::Deflation::saveVectors(), quda::MG::saveVectors(), quda::LatticeField::scatter(), quda::cudaColorSpinorField::sendGhost(), quda::cudaColorSpinorField::sendStart(), set_layout(), set_params(), quda::setDiracParam(), quda::cudaGaugeField::setGauge(), quda::cpuGaugeField::setGauge(), anonymous_namespace{dslash_policy.cuh}::setMappedGhost(), quda::Transfer::setSiteSubset(), quda::LatticeField::setTuningString(), quda::ColorSpinorField::setTuningString(), GaugeAlgTest::SetUp(), quda::shiftColorSpinorField(), quda::CG::solve(), quda::colorspinor::SpaceColorSpinorOrder< Float, Ns, Nc >::SpaceColorSpinorOrder(), quda::colorspinor::SpaceSpinorColorOrder< Float, Ns, Nc >::SpaceSpinorColorOrder(), quda::spinorGauss(), quda::staggeredDslashCuda(), staggeredDslashRef(), staggeredPhaseQuda(), quda::Timer::Start(), quda::Timer::Stop(), quda::STOUTStep(), test(), quda::gauge::TIFROrder< Float, length >::TIFROrder(), tmc_matpc(), quda::Transfer::Transfer(), quda::CalculateY< from_coarse, Float, fineSpin, fineColor, coarseSpin, coarseColor, Arg >::tuneKey(), quda::tuneLaunch(), quda::twistedCloverDslashCuda(), quda::twistedMassDslashCuda(), unbindSpinorTex(), unitarize_link_test(), quda::unitarizeLinks(), quda::cpuColorSpinorField::unpackGhost(), quda::cudaColorSpinorField::unpackGhostExtended(), quda::updateGaugeField(), updateGaugeFieldQuda(), quda::updateMomentum(), quda::GMResDR::UpdateSolution(), quda::Deflation::verify(), quda::MG::verify(), wil_dslash(), quda::wilsonDslashCuda(), quda::LatticeField::write(), write_field(), write_spinor_field(), quda::Tunable::writeAuxString(), quda::blas::xpayCpu(), quda::blas::xpyCpu(), and quda::cpuGaugeField::~cpuGaugeField().

printfQuda

#define printfQuda

(

...

)

Value:

do {                         \
  fprintf(getOutputFile(), "%s", getOutputPrefix()); \
  fprintf(getOutputFile(), __VA_ARGS__);             \
  fflush(getOutputFile());                           \
} while (0)

Definition at line 84 of file util_quda.h.

Referenced by quda::aligned_malloc(), quda::RNG::AllocateRNG(), quda::ArpackArgs< Float >::apply(), apply_staggered_phase_quda_(), quda::assertAllMemFree(), quda::RNG::backup(), quda::cublas::BatchInvertMatrix(), quda::calculateY(), closeMagma(), cloverQuda(), comm_declare_receive_relative_(), comm_declare_send_relative_(), comm_declare_strided_receive_relative_(), comm_declare_strided_send_relative_(), comm_peer2peer_init(), compare_mom(), compareFloats(), compareLink(), quda::compareSpinor(), quda::computeBeta(), covdevRef(), quda::Dirac::create(), quda::cudaColorSpinorField::create(), quda::ColorSpinorField::createGhostZone(), quda::MG::createSmoother(), quda::deflated_solver::deflated_solver(), quda::Deflation::Deflation(), quda::device_free_(), quda::device_malloc_(), quda::device_pinned_free_(), quda::device_pinned_malloc_(), display_test_info(), dslashCUDA(), dslashQuda(), dslashQuda_4dpc(), dslashQuda_mdwf(), dslashRef(), dslashTest(), quda::IncEigCG::eigCGsolve(), quda::EigParam::EigParam(), endQuda(), gauge_force_test(), quda::MG::generateNullVectors(), get_prec(), quda::cudaColorSpinorField::getTexObjectInfo(), hisq_force_test(), quda::host_free_(), quda::IncEigCG::IncEigCG(), quda::Deflation::increment(), init(), quda::IncEigCG::initCGsolve(), initComms(), initQudaDevice(), invert_test(), invertMultiShiftQuda(), invertMultiSrcQuda(), invertQuda(), lanczosQuda(), llfat_test(), loadCloverQuda(), loadGaugeQuda(), quda::loadTuneCache(), quda::Deflation::loadVectors(), quda::MG::loadVectors(), main(), quda::mapped_malloc_(), quda::massRescale(), MatDagMatQuda(), MatQuda(), quda::MG::MG(), quda::multigrid_solver::multigrid_solver(), open_test_input(), open_test_output(), openMagma(), OpenMagma(), quda::Lanczos::operator()(), quda::Deflation::operator()(), quda::MG::operator()(), quda::CG::operator()(), quda::MPCG::operator()(), quda::PreconCG::operator()(), quda::BiCGstab::operator()(), quda::SimpleBiCGstab::operator()(), quda::MPBiCGstab::operator()(), quda::BiCGstabL::operator()(), quda::GCR::operator()(), quda::MR::operator()(), quda::SD::operator()(), quda::MultiShiftCG::operator()(), quda::MinResExt::operator()(), quda::IncEigCG::operator()(), quda::GMResDR::operator()(), performAPEnStep(), performOvrImpSTOUTnStep(), performSTOUTnStep(), performWuppertalnStep(), quda::pinned_malloc_(), quda::DiracParam::print(), quda::EigParam::print(), DslashParam::print(), quda::ColorSpinorParam::print(), quda::TimeProfile::Print(), quda::print_alloc(), quda::print_alloc_header(), quda::print_trace(), quda::ColorSpinorField::PrintDims(), quda::TimeProfile::PrintGlobal(), printMomElement(), quda::printPeakMemUsage(), printQudaEigParam(), printQudaGaugeParam(), printQudaInvertParam(), printQudaMultigridParam(), quda::Solver::PrintStats(), quda::Solver::PrintSummary(), printVector(), process_command_line_option(), quda::qudaMemcpy_(), read_field(), read_gauge_field(), read_spinor_field(), quda::Deflation::reduce(), quda::RNG::Release(), remove_staggered_phase_quda_(), quda::report(), quda::Timer::Reset(), quda::ColorSpinorField::reset(), quda::RNG::restore(), quda::RNG::RNG(), quda::safe_malloc_(), quda::ArpackArgs< Float >::save(), quda::saveProfile(), quda::saveTuneCache(), quda::Deflation::saveVectors(), quda::MG::saveVectors(), set_layout(), setInvertParam(), setMultigridParam(), setNumaAffinityNVML(), quda::EigParam::setPrecision(), GaugeAlgTest::SetUp(), quda::CG::solve(), staggeredDslashRef(), quda::Timer::Start(), quda::Timer::Stop(), strong_check_link(), strong_check_mom(), SU3test(), GaugeAlgTest::TearDown(), TEST_F(), TEST_P(), total_staple_io_flops(), quda::Transfer::Transfer(), quda::tuneLaunch(), unitarize_link_test(), usage_extra(), quda::Deflation::verify(), quda::MG::verify(), write_field(), and write_spinor_field().

printfZero

#define printfZero

(

...

)

Value:

do {            \
    if (zeroThread) printf(__VA_ARGS__);        \
  } while (0)

Definition at line 42 of file util_quda.h.

warningQuda

#define warningQuda

(

...

)

Value:

do {                                 \
  if (getVerbosity() > QUDA_SILENT) {           \
    fprintf(getOutputFile(), "%sWARNING: ", getOutputPrefix()); \
    fprintf(getOutputFile(), __VA_ARGS__);                      \
    fprintf(getOutputFile(), "\n");                             \
    fflush(getOutputFile());                                    \
  }               \
} while (0)

Definition at line 101 of file util_quda.h.

Referenced by quda::assertAllMemFree(), quda::cublas::BatchInvertMatrix(), blasCuda(), quda::DiracClover::DiracClover(), anonymous_namespace{dslash_policy.cuh}::DslashPolicyTune::DslashPolicyTune(), dslashTest(), quda::IncEigCG::eigCGsolve(), quda::fillFGMResDRInnerSolveParam(), genericReduce(), quda::Deflation::increment(), quda::pool::init(), initCommsGridQuda(), initQudaDevice(), loadCloverQuda(), loadSloppyGaugeQuda(), quda::loadTuneCache(), main(), multiReduceCuda(), quda::CG::operator()(), quda::CGNE::operator()(), quda::PreconCG::operator()(), quda::BiCGstab::operator()(), quda::SimpleBiCGstab::operator()(), quda::MPBiCGstab::operator()(), quda::BiCGstabL::operator()(), quda::GCR::operator()(), quda::MultiShiftCG::operator()(), quda::IncEigCG::operator()(), quda::TimeProfile::Print(), quda::TimeProfile::PrintGlobal(), pushVerbosity(), reduceCuda(), quda::saveProfile(), quda::saveTuneCache(), setNumaAffinityNVML(), quda::CG::solve(), quda::SolverParam::SolverParam(), quda::Transfer::Transfer(), unitarize_link_test(), and quda::MG::verify().

zeroThread

#define zeroThread

Value:

(threadIdx.x + blockDim.x*blockIdx.x==0 &&    \
        threadIdx.y + blockDim.y*blockIdx.y==0 &&   \
        threadIdx.z + blockDim.z*blockIdx.z==0)

Definition at line 38 of file util_quda.h.

Function Documentation

getOutputFile()

FILE* getOutputFile

(

)

Definition at line 22 of file util_quda.cpp.

References outfile_.

getOutputPrefix()

char* getOutputPrefix

(

)

Definition at line 21 of file util_quda.cpp.

References prefix_.

getPrintBuffer()

char* getPrintBuffer

(

)

Definition at line 102 of file util_quda.cpp.

References buffer_.

getRankVerbosity()

bool getRankVerbosity

(

)

This function returns true if the calling rank is enabled for verbosity (e.g., whether printQuda and warningQuda will print out from this rank).

Returns

Return whether this rank will print

Definition at line 29 of file util_quda.cpp.

References comm_rank(), getenv(), and quda::blas::init().

Here is the call graph for this function:

getTuning()

QudaTune getTuning

(

)

Query whether autotuning is enabled or not. Default is enabled but can be overridden by setting QUDA_ENABLE_TUNING=0.

Returns

If autotuning is enabled

Definition at line 51 of file util_quda.cpp.

References getenv(), quda::blas::init(), QUDA_TUNE_NO, QUDA_TUNE_YES, strcmp(), and tune.

Referenced by quda::CopySpinor< FloatOut, FloatIn, Ns, Nc, OutOrder, InOrder >::apply(), quda::QudaMemCopy::apply(), quda::blas::copy_ns::CopyCuda< FloatN, N, Output, Input >::apply(), quda::GaussSpinor< FloatIn, Ns, Nc, InOrder >::apply(), BlasCuda< FloatN, M, SpinorX, SpinorY, SpinorZ, SpinorW, Functor >::apply(), quda::CopyGaugeEx< FloatOut, FloatIn, length, OutOrder, InOrder >::apply(), quda::GenericPackGhostLauncher< Float, Ns, Ms, Nc, Mc, Arg >::apply(), ReduceCuda< doubleN, ReduceType, FloatN, M, SpinorX, SpinorY, SpinorZ, SpinorW, SpinorV, Reducer >::apply(), quda::ShiftColorSpinorField< Output, Input >::apply(), quda::CopyColorSpinor< FloatOut, FloatIn, Ns, Nc, Arg >::apply(), quda::WuppertalSmearing< Float, Ns, Nc, Arg >::apply(), MultiBlasCuda< NXZ, FloatN, M, SpinorX, SpinorY, SpinorZ, SpinorW, Functor >::apply(), quda::Laplace< Float, nDim, nColor, Arg >::apply(), quda::ExtractGhost< Float, length, nDim, Order >::apply(), quda::ExtractGhostEx< Float, length, nDim, dim, Order >::apply(), quda::CopyGauge< FloatOut, FloatIn, length, OutOrder, InOrder, isGhost >::apply(), quda::CopyColorSpinor< FloatOut, FloatIn, 4, Nc, Arg >::apply(), quda::Gamma< ValueType, basis, dir >::apply(), quda::CopySpinorEx< FloatOut, FloatIn, Ns, Nc, OutOrder, InOrder, Basis, extend >::apply(), MultiReduceCuda< NXZ, doubleN, ReduceType, FloatN, M, SpinorX, SpinorY, SpinorZ, SpinorW, Reducer >::apply(), quda::TwistGamma< Float, nColor, Arg >::apply(), quda::blas::TileSizeTune< ReducerDiagonal, writeDiagonal, ReducerOffDiagonal, writeOffDiagonal >::apply(), quda::Clover< Float, nSpin, nColor, Arg >::apply(), quda::ProjectSU3< Float, G >::apply(), quda::TwistClover< Float, nSpin, nColor, Arg >::apply(), quda::GaugeOvrImpSTOUT< Float, GaugeOr, GaugeDs >::apply(), quda::DslashCoarsePolicyTune::apply(), quda::CalculateY< from_coarse, Float, fineSpin, fineColor, coarseSpin, coarseColor, Arg >::apply(), quda::CalculateYhat< Float, n, Arg >::apply(), anonymous_namespace{dslash_policy.cuh}::DslashPolicyTune::apply(), quda::DslashCoarsePolicyTune::DslashCoarsePolicyTune(), anonymous_namespace{dslash_policy.cuh}::DslashPolicyTune::DslashPolicyTune(), gauge_force_test(), quda::loadTuneCache(), and quda::blas::TileSizeTune< ReducerDiagonal, writeDiagonal, ReducerOffDiagonal, writeOffDiagonal >::TileSizeTune().

Here is the call graph for this function:

Here is the caller graph for this function:

getVerbosity()

QudaVerbosity getVerbosity

(

)

Definition at line 20 of file util_quda.cpp.

References verbosity_.

Referenced by quda::CopySpinor< FloatOut, FloatIn, Ns, Nc, OutOrder, InOrder >::apply(), quda::QudaMemCopy::apply(), quda::blas::copy_ns::CopyCuda< FloatN, N, Output, Input >::apply(), quda::GaussSpinor< FloatIn, Ns, Nc, InOrder >::apply(), BlasCuda< FloatN, M, SpinorX, SpinorY, SpinorZ, SpinorW, Functor >::apply(), quda::CopyGaugeEx< FloatOut, FloatIn, length, OutOrder, InOrder >::apply(), quda::GenericPackGhostLauncher< Float, Ns, Ms, Nc, Mc, Arg >::apply(), ReduceCuda< doubleN, ReduceType, FloatN, M, SpinorX, SpinorY, SpinorZ, SpinorW, SpinorV, Reducer >::apply(), quda::ShiftColorSpinorField< Output, Input >::apply(), quda::CopyColorSpinor< FloatOut, FloatIn, Ns, Nc, Arg >::apply(), quda::WuppertalSmearing< Float, Ns, Nc, Arg >::apply(), MultiBlasCuda< NXZ, FloatN, M, SpinorX, SpinorY, SpinorZ, SpinorW, Functor >::apply(), quda::Laplace< Float, nDim, nColor, Arg >::apply(), quda::ExtractGhost< Float, length, nDim, Order >::apply(), quda::ExtractGhostEx< Float, length, nDim, dim, Order >::apply(), quda::CopyGauge< FloatOut, FloatIn, length, OutOrder, InOrder, isGhost >::apply(), quda::CopyColorSpinor< FloatOut, FloatIn, 4, Nc, Arg >::apply(), quda::Gamma< ValueType, basis, dir >::apply(), quda::CopySpinorEx< FloatOut, FloatIn, Ns, Nc, OutOrder, InOrder, Basis, extend >::apply(), MultiReduceCuda< NXZ, doubleN, ReduceType, FloatN, M, SpinorX, SpinorY, SpinorZ, SpinorW, Reducer >::apply(), quda::TwistGamma< Float, nColor, Arg >::apply(), quda::blas::TileSizeTune< ReducerDiagonal, writeDiagonal, ReducerOffDiagonal, writeOffDiagonal >::apply(), quda::Clover< Float, nSpin, nColor, Arg >::apply(), quda::ProjectSU3< Float, G >::apply(), quda::TwistClover< Float, nSpin, nColor, Arg >::apply(), quda::GaugeOvrImpSTOUT< Float, GaugeOr, GaugeDs >::apply(), quda::CalculateYhat< Float, n, Arg >::apply(), apply_staggered_phase_quda_(), cloverQuda(), comm_gdr_blacklist(), comm_peer2peer_init(), quda::Dirac::create(), quda::cudaColorSpinorField::create(), quda::ColorSpinorField::createGhostZone(), quda::deflated_solver::deflated_solver(), quda::Deflation::Deflation(), anonymous_namespace{dslash_policy.cuh}::DslashPolicyTune::DslashPolicyTune(), dslashQuda(), dslashQuda_4dpc(), dslashQuda_mdwf(), endQuda(), quda::MG::generateNullVectors(), quda::Eig_Solver::GrandSchm_test(), quda::IncEigCG::initCGsolve(), initQudaDevice(), invertMultiShiftQuda(), invertMultiSrcQuda(), invertQuda(), lanczosQuda(), loadCloverQuda(), loadGaugeQuda(), quda::loadTuneCache(), quda::massRescale(), MatDagMatQuda(), MatQuda(), quda::MG::MG(), quda::multigrid_solver::multigrid_solver(), quda::CG::operator()(), quda::PreconCG::operator()(), quda::BiCGstab::operator()(), quda::BiCGstabL::operator()(), quda::GCR::operator()(), quda::MR::operator()(), quda::SD::operator()(), quda::MultiShiftCG::operator()(), quda::MinResExt::operator()(), quda::IncEigCG::operator()(), performAPEnStep(), performOvrImpSTOUTnStep(), performSTOUTnStep(), performWuppertalnStep(), quda::Solver::PrintStats(), quda::Solver::PrintSummary(), pushVerbosity(), quda::qudaMemcpy_(), quda::Deflation::reduce(), remove_staggered_phase_quda_(), quda::report(), quda::ColorSpinorField::reset(), quda::saveProfile(), quda::saveTuneCache(), quda::Transfer::Transfer(), quda::Deflation::~Deflation(), quda::Dirac::~Dirac(), and quda::MG::~MG().

popVerbosity()

void popVerbosity

(

)

Definition at line 93 of file util_quda.cpp.

References errorQuda, setVerbosity(), and vstack.

Referenced by cloverQuda(), dslashQuda(), dslashQuda_4dpc(), dslashQuda_mdwf(), quda::GMResDR::FlexArnoldiProcedure(), invertMultiShiftQuda(), invertMultiSrcQuda(), invertQuda(), lanczosQuda(), loadCloverQuda(), MatDagMatQuda(), MatQuda(), quda::GCR::operator()(), and performWuppertalnStep().

Here is the call graph for this function:

Here is the caller graph for this function:

pushVerbosity()

void pushVerbosity

(

QudaVerbosity

verbosity

)

Definition at line 82 of file util_quda.cpp.

References getVerbosity(), setVerbosity(), verbosity, vstack, and warningQuda.

Referenced by cloverQuda(), dslashQuda(), dslashQuda_4dpc(), dslashQuda_mdwf(), quda::GMResDR::FlexArnoldiProcedure(), invertMultiShiftQuda(), invertMultiSrcQuda(), invertQuda(), lanczosQuda(), loadCloverQuda(), MatDagMatQuda(), MatQuda(), quda::multigrid_solver::multigrid_solver(), quda::GCR::operator()(), and performWuppertalnStep().

Here is the call graph for this function:

Here is the caller graph for this function:

setOutputFile()

void setOutputFile

(

FILE *

outfile

)

Definition at line 74 of file util_quda.cpp.

References outfile_.

Referenced by setVerbosityQuda().

Here is the caller graph for this function:

setOutputPrefix()

void setOutputPrefix

(

const char *

prefix

)

Definition at line 68 of file util_quda.cpp.

References MAX_PREFIX_SIZE, prefix_, and strncpy().

Referenced by quda::MG::MG(), quda::MG::operator()(), quda::PreconditionedSolver::operator()(), setVerbosityQuda(), and quda::MG::verify().

Here is the call graph for this function:

Here is the caller graph for this function:

setVerbosity()

void setVerbosity

(

const QudaVerbosity

verbosity

)

Definition at line 24 of file util_quda.cpp.

References verbosity, and verbosity_.

Referenced by hisq_force_test(), init(), main(), popVerbosity(), pushVerbosity(), GaugeAlgTest::SetUp(), setVerbosityQuda(), and SU3test().

Here is the caller graph for this function: