CONFIG ?= config.mk
-include $(CONFIG)
COMMON ?= common.mk
-include $(COMMON)
ifeq (,$(filter-out undefined default,$(origin CC)))
CC = gcc
endif
ifeq (,$(filter-out undefined default,$(origin CXX)))
CXX = g++
endif
ifeq (,$(filter-out undefined default,$(origin FC)))
FC = gfortran
endif
ifeq (,$(filter-out undefined default,$(origin LINK)))
LINK = $(CC)
endif
ifeq (,$(filter-out undefined default,$(origin AR)))
AR = ar
endif
ifeq (,$(filter-out undefined default,$(origin ARFLAGS)))
ARFLAGS = crD
endif
NVCC ?= $(CUDA_DIR)/bin/nvcc
NVCC_CXX ?= $(CXX)
HIPCC ?= $(ROCM_DIR)/bin/hipcc
SYCLCXX ?= $(CXX)
SED ?= sed
ifneq ($(EMSCRIPTEN),)
STATIC = 1
EXE_SUFFIX = .wasm
EM_LDFLAGS = -s TOTAL_MEMORY=256MB
endif
ASAN ?=
CEED_LDFLAGS ?=
CEED_LDLIBS ?=
UNDERSCORE ?= 1
V ?= $(VERBOSE)
ifneq ($(wildcard ../mfem/libmfem.*),)
MFEM_DIR ?= ../mfem
endif
ifneq ($(wildcard ../Nek5000/*),)
NEK5K_DIR ?= $(abspath ../Nek5000)
endif
export NEK5K_DIR
MPI ?= 1
export CEED_DIR = $(abspath .)
XSMM_DIR ?= ../libxsmm
OCCA_DIR ?= ../occa/install
MAGMA_DIR ?= ../magma
CUDA_DIR ?=
CUDA_ARCH ?=
ROCM_DIR ?=
HIP_ARCH ?=
ifneq ($(wildcard ../petsc/lib/libpetsc.*),)
PETSC_DIR ?= ../petsc
endif
AFLAGS ?= -fsanitize=address
CC_VENDOR := $(firstword $(filter gcc (GCC) clang icc icc_orig oneAPI XL emcc,$(subst -, ,$(shell $(CC) --version))))
CC_VENDOR := $(subst (GCC),gcc,$(subst icc_orig,icc,$(CC_VENDOR)))
FC_VENDOR := $(if $(FC),$(firstword $(filter GNU ifort ifx XL,$(shell $(FC) --version 2>&1 || $(FC) -qversion))))
MARCHFLAG.gcc := -march=native
MARCHFLAG.clang := $(MARCHFLAG.gcc)
MARCHFLAG.icc :=
MARCHFLAG.oneAPI := $(MARCHFLAG.clang)
OMP_SIMD_FLAG.gcc := -fopenmp-simd
OMP_SIMD_FLAG.clang := $(OMP_SIMD_FLAG.gcc)
OMP_SIMD_FLAG.icc := -qopenmp-simd
OMP_SIMD_FLAG.oneAPI := $(OMP_SIMD_FLAG.icc)
OMP_FLAG.gcc := -fopenmp
OMP_FLAG.clang := $(OMP_FLAG.gcc)
OMP_FLAG.icc := -qopenmp
OMP_FLAG.oneAPI := $(OMP_FLAG.icc)
SYCL_FLAG.gcc :=
SYCL_FLAG.clang := -fsycl
SYCL_FLAG.icc :=
SYCL_FLAG.oneAPI := -fsycl -fno-sycl-id-queries-fit-in-int
OPT.gcc := -g -ffp-contract=fast
OPT.clang := $(OPT.gcc)
OPT.icc := $(OPT.gcc)
OPT.oneAPI := $(OPT.clang)
OPT.emcc :=
CFLAGS.gcc := $(if $(STATIC),,-fPIC) -std=c99 -Wall -Wextra -Wno-unused-parameter -MMD -MP
CFLAGS.clang := $(CFLAGS.gcc)
CFLAGS.icc := $(CFLAGS.gcc)
CFLAGS.oneAPI := $(CFLAGS.clang)
CFLAGS.XL := $(if $(STATIC),,-qpic) -MMD
CFLAGS.emcc := $(CFLAGS.clang)
CXXFLAGS.gcc := $(if $(STATIC),,-fPIC) -std=c++11 -Wall -Wextra -Wno-unused-parameter -MMD -MP
CXXFLAGS.clang := $(CXXFLAGS.gcc)
CXXFLAGS.icc := $(CXXFLAGS.gcc)
CXXFLAGS.oneAPI := $(CXXFLAGS.clang)
CXXFLAGS.XL := $(if $(STATIC),,-qpic) -std=c++11 -MMD
CXXFLAGS.emcc := $(CXXFLAGS.clang)
FFLAGS.GNU := $(if $(STATIC),,-fPIC) -cpp -Wall -Wextra -Wno-unused-parameter -Wno-unused-dummy-argument -MMD -MP
FFLAGS.ifort := $(if $(STATIC),,-fPIC) -cpp
FFLAGS.ifx := $(FFLAGS.ifort)
FFLAGS.XL := $(if $(STATIC),,-qpic) -ffree-form -qpreprocess -qextname -MMD
cc_check_flag = $(shell $(CC) -E -Werror $(1) -x c /dev/null > /dev/null 2>&1 && echo 1)
MARCHFLAG := $(MARCHFLAG.$(CC_VENDOR))
MARCHFLAG := $(if $(call cc_check_flag,$(MARCHFLAG)),$(MARCHFLAG),-mcpu=native)
MARCHFLAG := $(if $(call cc_check_flag,$(MARCHFLAG)),$(MARCHFLAG))
OMP_SIMD_FLAG := $(OMP_SIMD_FLAG.$(CC_VENDOR))
OMP_SIMD_FLAG := $(if $(call cc_check_flag,$(OMP_SIMD_FLAG)),$(OMP_SIMD_FLAG))
PEDANTIC ?=
PEDANTICFLAGS ?= -Werror -pedantic
OPT ?= -O $(MARCHFLAG) $(OPT.$(CC_VENDOR)) $(OMP_SIMD_FLAG)
CFLAGS ?= $(OPT) $(CFLAGS.$(CC_VENDOR)) $(if $(PEDANTIC),$(PEDANTICFLAGS))
CXXFLAGS ?= $(OPT) $(CXXFLAGS.$(CC_VENDOR)) $(if $(PEDANTIC),$(PEDANTICFLAGS))
FFLAGS ?= $(OPT) $(FFLAGS.$(FC_VENDOR))
LIBCXX ?= -lstdc++
NVCCFLAGS ?= -ccbin $(CXX) -Xcompiler "$(OPT)" -Xcompiler -fPIC
ifneq ($(CUDA_ARCH),)
NVCCFLAGS += -arch=$(CUDA_ARCH)
endif
HIPCCFLAGS ?= $(filter-out $(OMP_SIMD_FLAG),$(OPT)) -fPIC -munsafe-fp-atomics
ifneq ($(HIP_ARCH),)
HIPCCFLAGS += --amdgpu-target=$(HIP_ARCH)
endif
SYCL_FLAG := $(SYCL_FLAG.$(CC_VENDOR))
SYCLFLAGS ?= $(SYCL_FLAG) -fPIC -std=c++17 $(filter-out -std=c++11,$(CXXFLAGS)) $(filter-out $(OMP_SIMD_FLAG),$(OPT))
OPENMP ?=
ifneq ($(OPENMP),)
OMP_FLAG := $(OMP_FLAG.$(CC_VENDOR))
OMP_FLAG := $(if $(call cc_check_flag,$(OMP_FLAG)),$(OMP_FLAG))
CFLAGS += $(OMP_FLAG)
CEED_LDFLAGS += $(OMP_FLAG)
endif
ifeq ($(COVERAGE), 1)
CFLAGS += --coverage
CXXFLAGS += --coverage
CEED_LDFLAGS += --coverage
endif
CFLAGS += $(if $(ASAN),$(AFLAGS))
FFLAGS += $(if $(ASAN),$(AFLAGS))
CEED_LDFLAGS += $(if $(ASAN),$(AFLAGS))
CPPFLAGS += -I./include
CEED_LDLIBS = -lm
OBJDIR := build
for_install := $(filter install,$(MAKECMDGOALS))
LIBDIR := $(if $(for_install),$(OBJDIR),lib)
prefix ?= /usr/local
bindir = $(prefix)/bin
libdir = $(prefix)/lib
includedir = $(prefix)/include
pkgconfigdir = $(libdir)/pkgconfig
INSTALL = install
INSTALL_PROGRAM = $(INSTALL)
INSTALL_DATA = $(INSTALL) -m644
NPROCS := $(shell getconf _NPROCESSORS_ONLN)
MFLAGS := -j $(NPROCS) --warn-undefined-variables \
--no-print-directory --no-keep-going
PYTHON ?= python3
PROVE ?= prove
PROVE_OPTS ?= -j $(NPROCS)
DARWIN := $(filter Darwin,$(shell uname -s))
SO_EXT := $(if $(DARWIN),dylib,so)
ceed.pc := $(LIBDIR)/pkgconfig/ceed.pc
libceed.so := $(LIBDIR)/libceed.$(SO_EXT)
libceed.a := $(LIBDIR)/libceed.a
libceed := $(if $(STATIC),$(libceed.a),$(libceed.so))
CEED_LIBS = -lceed
libceed.c := $(filter-out interface/ceed-cuda.c interface/ceed-hip.c interface/ceed-jit-source-root-$(if $(for_install),default,install).c, $(wildcard interface/ceed*.c backends/*.c gallery/*.c))
gallery.c := $(wildcard gallery/*/ceed*.c)
libceed.c += $(gallery.c)
libceeds = $(libceed)
BACKENDS_BUILTIN := /cpu/self/ref/serial /cpu/self/ref/blocked /cpu/self/opt/serial /cpu/self/opt/blocked
BACKENDS_MAKE := $(BACKENDS_BUILTIN)
TEST_BACKENDS := /cpu/self/tmpl /cpu/self/tmpl/sub
tests.c := $(sort $(wildcard tests/t[0-9][0-9][0-9]-*.c))
tests.f := $(if $(FC),$(sort $(wildcard tests/t[0-9][0-9][0-9]-*.f90)))
tests := $(tests.c:tests/%.c=$(OBJDIR)/%$(EXE_SUFFIX))
ctests := $(tests)
tests += $(tests.f:tests/%.f90=$(OBJDIR)/%$(EXE_SUFFIX))
examples.c := $(sort $(wildcard examples/ceed/*.c))
examples.f := $(if $(FC),$(sort $(wildcard examples/ceed/*.f)))
examples := $(examples.c:examples/ceed/%.c=$(OBJDIR)/%$(EXE_SUFFIX))
examples += $(examples.f:examples/ceed/%.f=$(OBJDIR)/%$(EXE_SUFFIX))
mfemexamples.cpp := $(sort $(wildcard examples/mfem/*.cpp))
mfemexamples := $(mfemexamples.cpp:examples/mfem/%.cpp=$(OBJDIR)/mfem-%)
nekexamples := $(OBJDIR)/nek-bps
petscexamples.c := $(wildcard examples/petsc/*.c)
petscexamples := $(petscexamples.c:examples/petsc/%.c=$(OBJDIR)/petsc-%)
fluidsexamples.c := $(sort $(wildcard examples/fluids/*.c))
fluidsexamples := $(fluidsexamples.c:examples/fluids/%.c=$(OBJDIR)/fluids-%)
solidsexamples.c := $(sort $(wildcard examples/solids/*.c))
solidsexamples := $(solidsexamples.c:examples/solids/%.c=$(OBJDIR)/solids-%)
ref.c := $(sort $(wildcard backends/ref/*.c))
blocked.c := $(sort $(wildcard backends/blocked/*.c))
ceedmemcheck.c := $(sort $(wildcard backends/memcheck/*.c))
opt.c := $(sort $(wildcard backends/opt/*.c))
avx.c := $(sort $(wildcard backends/avx/*.c))
xsmm.c := $(sort $(wildcard backends/xsmm/*.c))
cuda.c := $(sort $(wildcard backends/cuda/*.c))
cuda.cpp := $(sort $(wildcard backends/cuda/*.cpp))
cuda-ref.c := $(sort $(wildcard backends/cuda-ref/*.c))
cuda-ref.cpp := $(sort $(wildcard backends/cuda-ref/*.cpp))
cuda-ref.cu := $(sort $(wildcard backends/cuda-ref/kernels/*.cu))
cuda-shared.c := $(sort $(wildcard backends/cuda-shared/*.c))
cuda-shared.cu := $(sort $(wildcard backends/cuda-shared/kernels/*.cu))
cuda-gen.c := $(sort $(wildcard backends/cuda-gen/*.c))
cuda-gen.cpp := $(sort $(wildcard backends/cuda-gen/*.cpp))
cuda-gen.cu := $(sort $(wildcard backends/cuda-gen/kernels/*.cu))
occa.cpp := $(sort $(shell find backends/occa -type f -name *.cpp))
magma.c := $(sort $(wildcard backends/magma/*.c))
magma.cpp := $(sort $(wildcard backends/magma/*.cpp))
hip.c := $(sort $(wildcard backends/hip/*.c))
hip.cpp := $(sort $(wildcard backends/hip/*.cpp))
hip-ref.c := $(sort $(wildcard backends/hip-ref/*.c))
hip-ref.cpp := $(sort $(wildcard backends/hip-ref/*.cpp))
hip-ref.hip := $(sort $(wildcard backends/hip-ref/kernels/*.hip.cpp))
hip-shared.c := $(sort $(wildcard backends/hip-shared/*.c))
hip-gen.c := $(sort $(wildcard backends/hip-gen/*.c))
hip-gen.cpp := $(sort $(wildcard backends/hip-gen/*.cpp))
sycl-core.cpp := $(sort $(wildcard backends/sycl/*.sycl.cpp))
sycl-ref.cpp := $(sort $(wildcard backends/sycl-ref/*.sycl.cpp))
sycl-shared.cpp:= $(sort $(wildcard backends/sycl-shared/*.sycl.cpp))
sycl-gen.cpp := $(sort $(wildcard backends/sycl-gen/*.sycl.cpp))
hip-all.c := interface/ceed-hip.c $(hip.c) $(hip-ref.c) $(hip-shared.c) $(hip-gen.c)
hip-all.cpp := $(hip.cpp) $(hip-ref.cpp) $(hip-gen.cpp)
quiet ?= $($(1))
.SUFFIXES:
.SECONDEXPANSION:
%/.DIR :
@mkdir -p $(@D)
@touch $@
.PRECIOUS: %/.DIR
lib: $(libceed) $(ceed.pc)
par:;@$(MAKE) $(MFLAGS) V=$(V) lib
backend_status = $(if $(filter $1,$(BACKENDS_MAKE)), [backends: $1], [not found])
info:
$(info ------------------------------------)
$(info CC = $(CC))
$(info CXX = $(CXX))
$(info FC = $(FC))
$(info CPPFLAGS = $(CPPFLAGS))
$(info CFLAGS = $(CFLAGS))
$(info CXXFLAGS = $(CXXFLAGS))
$(info FFLAGS = $(FFLAGS))
$(info NVCCFLAGS = $(NVCCFLAGS))
$(info HIPCCFLAGS = $(HIPCCFLAGS))
$(info SYCLFLAGS = $(SYCLFLAGS))
$(info CEED_LDFLAGS = $(CEED_LDFLAGS))
$(info CEED_LDLIBS = $(CEED_LDLIBS))
$(info AR = $(AR))
$(info ARFLAGS = $(ARFLAGS))
$(info OPT = $(OPT))
$(info AFLAGS = $(AFLAGS))
$(info ASAN = $(or $(ASAN),(empty)))
$(info VERBOSE = $(or $(V),(empty)) [verbose=$(if $(V),on,off)])
$(info ------------------------------------)
$(info MEMCHK_STATUS = $(MEMCHK_STATUS)$(call backend_status,$(MEMCHK_BACKENDS)))
$(info AVX_STATUS = $(AVX_STATUS)$(call backend_status,$(AVX_BACKENDS)))
$(info XSMM_DIR = $(XSMM_DIR)$(call backend_status,$(XSMM_BACKENDS)))
$(info OCCA_DIR = $(OCCA_DIR)$(call backend_status,$(OCCA_BACKENDS)))
$(info MAGMA_DIR = $(MAGMA_DIR)$(call backend_status,$(MAGMA_BACKENDS)))
$(info CUDA_DIR = $(CUDA_DIR)$(call backend_status,$(CUDA_BACKENDS)))
$(info ROCM_DIR = $(ROCM_DIR)$(call backend_status,$(HIP_BACKENDS)))
$(info SYCL_DIR = $(SYCL_DIR)$(call backend_status,$(SYCL_BACKENDS)))
$(info ------------------------------------)
$(info MFEM_DIR = $(MFEM_DIR))
$(info NEK5K_DIR = $(NEK5K_DIR))
$(info PETSC_DIR = $(PETSC_DIR))
$(info ------------------------------------)
$(info prefix = $(prefix))
$(info includedir = $(value includedir))
$(info libdir = $(value libdir))
$(info pkgconfigdir = $(value pkgconfigdir))
$(info ------------------------------------)
@true
info-backends:
$(info make: 'lib' with optional backends: $(filter-out $(BACKENDS_BUILTIN),$(BACKENDS)))
@true
info-backends-all:
$(info make: 'lib' with backends: $(filter-out $(TEST_BACKENDS),$(BACKENDS)))
@true
$(libceed.so) : CEED_LDFLAGS += $(if $(DARWIN), -install_name @rpath/$(notdir $(libceed.so)))
libceed.c += $(ref.c)
libceed.c += $(blocked.c)
libceed.c += $(opt.c)
MEMCHK_STATUS = Disabled
MEMCHK := $(shell echo "$(HASH)include <valgrind/memcheck.h>" | $(CC) $(CPPFLAGS) -E - >/dev/null 2>&1 && echo 1)
MEMCHK_BACKENDS = /cpu/self/memcheck/serial /cpu/self/memcheck/blocked
ifeq ($(MEMCHK),1)
MEMCHK_STATUS = Enabled
libceed.c += $(ceedmemcheck.c)
BACKENDS_MAKE += $(MEMCHK_BACKENDS)
endif
AVX_STATUS = Disabled
AVX_FLAG := $(if $(filter clang,$(CC_VENDOR)),+avx,-mavx)
AVX := $(filter $(AVX_FLAG),$(shell $(CC) $(CFLAGS:-M%=) -v -E -x c /dev/null 2>&1))
AVX_BACKENDS = /cpu/self/avx/serial /cpu/self/avx/blocked
ifneq ($(AVX),)
AVX_STATUS = Enabled
libceed.c += $(avx.c)
BACKENDS_MAKE += $(AVX_BACKENDS)
endif
PKG_LIBS =
PKG_STUBS_LIBS =
XSMM_BACKENDS = /cpu/self/xsmm/serial /cpu/self/xsmm/blocked
ifneq ($(wildcard $(XSMM_DIR)/lib/libxsmm.*),)
PKG_LIBS += -L$(abspath $(XSMM_DIR))/lib -lxsmm
MKL ?=
ifeq (,$(MKL)$(MKLROOT))
BLAS_LIB ?= -lblas -ldl
else
ifneq ($(MKLROOT),)
MKL_LIBDIR = $(dir $(firstword $(wildcard $(MKLROOT)/lib/intel64/libmkl_sequential.* $(MKLROOT)/lib/libmkl_sequential.*)))
MKL_LINK = -L$(MKL_LIBDIR)
endif
BLAS_LIB ?= $(MKL_LINK) -Wl,--push-state,--no-as-needed -lmkl_intel_lp64 -lmkl_sequential -lmkl_core -lpthread -lm -ldl -Wl,--pop-state
endif
PKG_LIBS += $(BLAS_LIB)
libceed.c += $(xsmm.c)
$(xsmm.c:%.c=$(OBJDIR)/%.o) $(xsmm.c:%=%.tidy) : CPPFLAGS += -I$(XSMM_DIR)/include
BACKENDS_MAKE += $(XSMM_BACKENDS)
endif
OCCA_BACKENDS = /cpu/self/occa
ifneq ($(wildcard $(OCCA_DIR)/lib/libocca.*),)
OCCA_MODES := $(shell LD_LIBRARY_PATH=$(OCCA_DIR)/lib $(OCCA_DIR)/bin/occa modes)
OCCA_BACKENDS += $(if $(filter OpenMP,$(OCCA_MODES)),/cpu/openmp/occa)
OCCA_BACKENDS += $(if $(filter dpcpp,$(OCCA_MODES)),/gpu/dpcpp/occa)
OCCA_BACKENDS += $(if $(filter OpenCL,$(OCCA_MODES)),/gpu/opencl/occa)
OCCA_BACKENDS += $(if $(filter HIP,$(OCCA_MODES)),/gpu/hip/occa)
OCCA_BACKENDS += $(if $(filter CUDA,$(OCCA_MODES)),/gpu/cuda/occa)
$(libceeds) : CPPFLAGS += -I$(OCCA_DIR)/include
PKG_LIBS += -L$(abspath $(OCCA_DIR))/lib -locca
LIBCEED_CONTAINS_CXX = 1
libceed.cpp += $(occa.cpp)
BACKENDS_MAKE += $(OCCA_BACKENDS)
endif
ifneq ($(CUDA_DIR),)
CUDA_LIB_DIR := $(wildcard $(foreach d,lib lib64 lib/x86_64-linux-gnu,$(CUDA_DIR)/$d/libcudart.${SO_EXT}))
CUDA_LIB_DIR := $(patsubst %/,%,$(dir $(firstword $(CUDA_LIB_DIR))))
endif
CUDA_LIB_DIR_STUBS := $(CUDA_LIB_DIR)/stubs
CUDA_BACKENDS = /gpu/cuda/ref /gpu/cuda/shared /gpu/cuda/gen
ifneq ($(CUDA_LIB_DIR),)
$(libceeds) : CPPFLAGS += -I$(CUDA_DIR)/include
PKG_LIBS += -L$(abspath $(CUDA_LIB_DIR)) -lcudart -lnvrtc -lcuda -lcublas
PKG_STUBS_LIBS += -L$(CUDA_LIB_DIR_STUBS)
LIBCEED_CONTAINS_CXX = 1
libceed.c += interface/ceed-cuda.c
libceed.c += $(cuda.c) $(cuda-ref.c) $(cuda-shared.c) $(cuda-gen.c)
libceed.cpp += $(cuda.cpp) $(cuda-ref.cpp) $(cuda-gen.cpp)
libceed.cu += $(cuda-ref.cu) $(cuda-shared.cu) $(cuda-gen.cu)
BACKENDS_MAKE += $(CUDA_BACKENDS)
endif
HIP_LIB_DIR := $(wildcard $(foreach d,lib lib64,$(ROCM_DIR)/$d/libamdhip64.${SO_EXT}))
HIP_LIB_DIR := $(patsubst %/,%,$(dir $(firstword $(HIP_LIB_DIR))))
HIP_BACKENDS = /gpu/hip/ref /gpu/hip/shared /gpu/hip/gen
ifneq ($(HIP_LIB_DIR),)
HIPCONFIG_CPPFLAGS := $(subst =,,$(shell $(ROCM_DIR)/bin/hipconfig -C))
$(hip-all.c:%.c=$(OBJDIR)/%.o) $(hip-all.c:%=%.tidy): CPPFLAGS += $(HIPCONFIG_CPPFLAGS)
ifneq ($(CXX), $(HIPCC))
$(hip-all.cpp:%.cpp=$(OBJDIR)/%.o) $(hip-all.cpp:%=%.tidy): CPPFLAGS += $(HIPCONFIG_CPPFLAGS)
endif
PKG_LIBS += -L$(abspath $(HIP_LIB_DIR)) -lamdhip64 -lhipblas
LIBCEED_CONTAINS_CXX = 1
libceed.c += $(hip-all.c)
libceed.cpp += $(hip-all.cpp)
libceed.hip += $(hip-ref.hip)
BACKENDS_MAKE += $(HIP_BACKENDS)
endif
SYCL_BACKENDS = /gpu/sycl/ref /gpu/sycl/shared /gpu/sycl/gen
ifneq ($(SYCL_DIR),)
SYCL_LIB_DIR := $(wildcard $(foreach d,lib lib64,$(SYCL_DIR)/$d/libsycl.${SO_EXT}))
SYCL_LIB_DIR := $(patsubst %/,%,$(dir $(firstword $(SYCL_LIB_DIR))))
endif
ifneq ($(SYCL_LIB_DIR),)
PKG_LIBS += $(SYCL_FLAG) -lze_loader
LIBCEED_CONTAINS_CXX = 1
libceed.sycl += $(sycl-core.cpp) $(sycl-ref.cpp) $(sycl-shared.cpp) $(sycl-gen.cpp)
BACKENDS_MAKE += $(SYCL_BACKENDS)
endif
ifneq ($(wildcard $(MAGMA_DIR)/lib/libmagma.*),)
MAGMA_ARCH=$(shell nm -g $(MAGMA_DIR)/lib/libmagma.* | grep -c "hipblas")
ifeq ($(MAGMA_ARCH), 0) # CUDA MAGMA
ifneq ($(CUDA_LIB_DIR),)
cuda_link = $(if $(STATIC),,-Wl,-rpath,$(CUDA_LIB_DIR)) -L$(CUDA_LIB_DIR) -lcublas -lcusparse -lcudart
omp_link = -fopenmp
magma_link_static = -L$(MAGMA_DIR)/lib -lmagma $(cuda_link) $(omp_link)
magma_link_shared = -L$(MAGMA_DIR)/lib $(if $(STATIC),,-Wl,-rpath,$(abspath $(MAGMA_DIR)/lib)) -lmagma
magma_link := $(if $(wildcard $(MAGMA_DIR)/lib/libmagma.${SO_EXT}),$(magma_link_shared),$(magma_link_static))
PKG_LIBS += $(magma_link)
libceed.c += $(magma.c)
libceed.cpp += $(magma.cpp)
$(magma.c:%.c=$(OBJDIR)/%.o) $(magma.c:%=%.tidy) : CPPFLAGS += -DADD_ -I$(MAGMA_DIR)/include -I$(CUDA_DIR)/include
$(magma.cpp:%.cpp=$(OBJDIR)/%.o) $(magma.cpp:%=%.tidy) : CPPFLAGS += -DADD_ -I$(MAGMA_DIR)/include -I$(CUDA_DIR)/include
MAGMA_BACKENDS = /gpu/cuda/magma /gpu/cuda/magma/det
endif
else ifneq ($(HIP_LIB_DIR),)
omp_link = -fopenmp
hip_link = $(if $(STATIC),,-Wl,-rpath,$(HIP_LIB_DIR)) -L$(HIP_LIB_DIR) -lhipblas -lhipsparse -lamdhip64
magma_link_static = -L$(MAGMA_DIR)/lib -lmagma $(hip_link) $(omp_link)
magma_link_shared = -L$(MAGMA_DIR)/lib $(hip_link) $(omp_link) $(if $(STATIC),,-Wl,-rpath,$(abspath $(MAGMA_DIR)/lib)) -lmagma
magma_link := $(if $(wildcard $(MAGMA_DIR)/lib/libmagma.${SO_EXT}),$(magma_link_shared),$(magma_link_static))
PKG_LIBS += $(magma_link)
libceed.c += $(magma.c)
libceed.cpp += $(magma.cpp)
$(magma.c:%.c=$(OBJDIR)/%.o) $(magma.c:%=%.tidy) : CPPFLAGS += $(HIPCONFIG_CPPFLAGS) -I$(MAGMA_DIR)/include -I$(ROCM_DIR)/include -DCEED_MAGMA_USE_HIP -DADD_
$(magma.cpp:%.cpp=$(OBJDIR)/%.o) $(magma.cpp:%=%.tidy) : CPPFLAGS += $(HIPCONFIG_CPPFLAGS) -I$(MAGMA_DIR)/include -I$(ROCM_DIR)/include -DCEED_MAGMA_USE_HIP -DADD_
MAGMA_BACKENDS = /gpu/hip/magma /gpu/hip/magma/det
endif
endif
LIBCEED_CONTAINS_CXX = 1
BACKENDS_MAKE += $(MAGMA_BACKENDS)
endif
BACKENDS ?= $(BACKENDS_MAKE)
export BACKENDS
_pkg_ldflags = $(filter -L%,$(PKG_LIBS))
_pkg_ldlibs = $(filter-out -L%,$(PKG_LIBS))
$(libceeds) : CEED_LDFLAGS += $(_pkg_ldflags) $(if $(STATIC),,$(_pkg_ldflags:-L%=-Wl,-rpath,%)) $(PKG_STUBS_LIBS)
$(libceeds) : CEED_LDLIBS += $(_pkg_ldlibs)
ifeq ($(STATIC),1)
$(examples) $(tests) : CEED_LDFLAGS += $(EM_LDFLAGS) $(_pkg_ldflags) $(if $(STATIC),,$(_pkg_ldflags:-L%=-Wl,-rpath,%)) $(PKG_STUBS_LIBS)
$(examples) $(tests) : CEED_LDLIBS += $(_pkg_ldlibs)
endif
pkgconfig-libs-private = $(PKG_LIBS)
ifeq ($(LIBCEED_CONTAINS_CXX),1)
$(libceeds) : LINK = $(CXX)
ifeq ($(STATIC),1)
$(examples) $(tests) : CEED_LDLIBS += $(LIBCXX)
pkgconfig-libs-private += $(LIBCXX)
endif
endif
weak_last = $(filter-out %-weak.o,$(1)) $(filter %-weak.o,$(1))
libceed.o = $(libceed.c:%.c=$(OBJDIR)/%.o) $(libceed.cpp:%.cpp=$(OBJDIR)/%.o) $(libceed.cu:%.cu=$(OBJDIR)/%.o) $(libceed.hip:%.hip.cpp=$(OBJDIR)/%.o) $(libceed.sycl:%.sycl.cpp=$(OBJDIR)/%.o)
$(filter %fortran.o,$(libceed.o)) : CPPFLAGS += $(if $(filter 1,$(UNDERSCORE)),-DUNDERSCORE)
$(libceed.o): | info-backends
$(libceed.so) : $(call weak_last,$(libceed.o)) | $$(@D)/.DIR
$(call quiet,LINK) $(LDFLAGS) $(CEED_LDFLAGS) -shared -o $@ $^ $(CEED_LDLIBS) $(LDLIBS)
$(libceed.a) : $(call weak_last,$(libceed.o)) | $$(@D)/.DIR
$(call quiet,AR) $(ARFLAGS) $@ $^
$(OBJDIR)/%.o : $(CURDIR)/%.c | $$(@D)/.DIR
$(call quiet,CC) $(CPPFLAGS) $(CFLAGS) -c -o $@ $(abspath $<)
$(OBJDIR)/%.o : $(CURDIR)/%.cpp | $$(@D)/.DIR
$(call quiet,CXX) $(CPPFLAGS) $(CXXFLAGS) -c -o $@ $(abspath $<)
$(OBJDIR)/%.o : $(CURDIR)/%.cu | $$(@D)/.DIR
$(call quiet,NVCC) $(filter-out -Wno-unused-function, $(CPPFLAGS)) $(NVCCFLAGS) -c -o $@ $(abspath $<)
$(OBJDIR)/%.o : $(CURDIR)/%.hip.cpp | $$(@D)/.DIR
$(call quiet,HIPCC) $(CPPFLAGS) $(HIPCCFLAGS) -c -o $@ $(abspath $<)
$(OBJDIR)/%.o : $(CURDIR)/%.sycl.cpp | $$(@D)/.DIR
$(call quiet,SYCLCXX) $(SYCLFLAGS) $(CPPFLAGS) -c -o $@ $(abspath $<)
$(OBJDIR)/%.o : $(CURDIR)/%.sycl.cpp | $$(@D)/.DIR
$(call quiet,SYCLCXX) $(SYCLFLAGS) $(CPPFLAGS) -c -o $@ $(abspath $<)
$(OBJDIR)/%$(EXE_SUFFIX) : tests/%.c | $$(@D)/.DIR
$(call quiet,LINK.c) $(CEED_LDFLAGS) -o $@ $(abspath $<) $(CEED_LIBS) $(CEED_LDLIBS) $(LDLIBS)
$(OBJDIR)/%$(EXE_SUFFIX) : tests/%.f90 | $$(@D)/.DIR
$(call quiet,LINK.F) -DSOURCE_DIR='"$(abspath $(<D))/"' $(CEED_LDFLAGS) -o $@ $(abspath $<) $(CEED_LIBS) $(CEED_LDLIBS) $(LDLIBS)
$(OBJDIR)/%$(EXE_SUFFIX) : examples/ceed/%.c | $$(@D)/.DIR
$(call quiet,LINK.c) $(CEED_LDFLAGS) -o $@ $(abspath $<) $(CEED_LIBS) $(CEED_LDLIBS) $(LDLIBS)
$(OBJDIR)/%$(EXE_SUFFIX) : examples/ceed/%.f | $$(@D)/.DIR
$(call quiet,LINK.F) -DSOURCE_DIR='"$(abspath $(<D))/"' $(CEED_LDFLAGS) -o $@ $(abspath $<) $(CEED_LIBS) $(CEED_LDLIBS) $(LDLIBS)
$(OBJDIR)/mfem-% : examples/mfem/%.cpp $(libceed) | $$(@D)/.DIR
+$(MAKE) -C examples/mfem CEED_DIR=`pwd` \
MFEM_DIR="$(abspath $(MFEM_DIR))" CXX=$(CXX) $*
cp examples/mfem/$* $@
$(OBJDIR)/nek-bps : examples/nek/bps/bps.usr examples/nek/nek-examples.sh $(libceed) | $$(@D)/.DIR
+$(MAKE) -C examples MPI=$(MPI) CEED_DIR=`pwd` NEK5K_DIR="$(abspath $(NEK5K_DIR))" nek
mv examples/nek/build/bps $(OBJDIR)/bps
cp examples/nek/nek-examples.sh $(OBJDIR)/nek-bps
examples/petsc/libutils.a.PHONY: $(libceed) $(ceed.pc)
+$(call quiet,MAKE) -C examples/petsc CEED_DIR=`pwd` AR=$(AR) ARFLAGS=$(ARFLAGS) \
PETSC_DIR="$(abspath $(PETSC_DIR))" OPT="$(OPT)" $(basename $(@F))
$(OBJDIR)/petsc-% : examples/petsc/%.c examples/petsc/libutils.a.PHONY $(libceed) $(ceed.pc) | $$(@D)/.DIR
+$(call quiet,MAKE) -C examples/petsc CEED_DIR=`pwd` \
PETSC_DIR="$(abspath $(PETSC_DIR))" OPT="$(OPT)" $*
cp examples/petsc/$* $@
$(OBJDIR)/fluids-% : examples/fluids/%.c examples/fluids/src/*.c examples/fluids/*.h examples/fluids/problems/*.c examples/fluids/qfunctions/*.h $(libceed) $(ceed.pc) | $$(@D)/.DIR
+$(call quiet,MAKE) -C examples/fluids CEED_DIR=`pwd` \
PETSC_DIR="$(abspath $(PETSC_DIR))" OPT="$(OPT)" $*
cp examples/fluids/$* $@
$(OBJDIR)/solids-% : examples/solids/%.c examples/solids/%.h \
examples/solids/problems/*.c examples/solids/src/*.c \
examples/solids/include/*.h examples/solids/problems/*.h examples/solids/qfunctions/*.h \
$(libceed) $(ceed.pc) | $$(@D)/.DIR
+$(call quiet,MAKE) -C examples/solids CEED_DIR=`pwd` \
PETSC_DIR="$(abspath $(PETSC_DIR))" OPT="$(OPT)" $*
cp examples/solids/$* $@
$(examples) : $(libceed)
$(tests) : $(libceed)
$(tests) $(examples) : override LDFLAGS += $(if $(STATIC),,-Wl,-rpath,$(abspath $(LIBDIR))) -L$(LIBDIR)
NPROC_TEST ?= 1
export NPROC_TEST
NPROC_POOL ?= 1
export NPROC_POOL
run-% : $(OBJDIR)/%
@$(PYTHON) tests/junit.py --mode tap --ceed-backends $(BACKENDS) --nproc $(NPROC_TEST) --pool-size $(NPROC_POOL) $(<:$(OBJDIR)/%=%)
external_examples := \
$(if $(MFEM_DIR),$(mfemexamples)) \
$(if $(PETSC_DIR),$(petscexamples)) \
$(if $(NEK5K_DIR),$(nekexamples)) \
$(if $(PETSC_DIR),$(fluidsexamples)) \
$(if $(PETSC_DIR),$(solidsexamples))
allexamples = $(examples) $(external_examples)
search ?= t ex
realsearch = $(search:%=%%)
matched = $(foreach pattern,$(realsearch),$(filter $(OBJDIR)/$(pattern),$(tests) $(allexamples)))
JUNIT_BATCH ?= ''
test : $(matched:$(OBJDIR)/%=run-%)
tst : ;@$(MAKE) $(MFLAGS) V=$(V) test
ctc-% : $(ctests);@$(foreach tst,$(ctests),$(tst) /cpu/$*;)
prove : $(matched)
$(info Testing backends: $(BACKENDS))
$(PROVE) $(PROVE_OPTS) --exec 'tests/junit.py --mode tap --ceed-backends $(BACKENDS) --nproc $(NPROC_TEST) --pool-size $(NPROC_POOL)' $(matched:$(OBJDIR)/%=%)
prv : ;@$(MAKE) $(MFLAGS) V=$(V) prove
prove-all :
+$(MAKE) prove realsearch=%
junit-% : $(OBJDIR)/%
@printf " %10s %s\n" TEST $(<:$(OBJDIR)/%=%); $(PYTHON) tests/junit.py --ceed-backends $(BACKENDS) --nproc $(NPROC_TEST) --pool-size $(NPROC_POOL) --junit-batch $(JUNIT_BATCH) $(<:$(OBJDIR)/%=%)
junit : $(matched:$(OBJDIR)/%=junit-%)
all: $(alltests)
examples : $(allexamples)
ceedexamples : $(examples)
nekexamples : $(nekexamples)
mfemexamples : $(mfemexamples)
petscexamples : $(petscexamples)
allbenchmarks = petsc-bps
bench_targets = $(addprefix bench-,$(allbenchmarks))
.PHONY: $(bench_targets) benchmarks
$(bench_targets): bench-%: $(OBJDIR)/%
cd benchmarks && ./benchmark.sh --ceed "$(BACKENDS_MAKE)" -r $(*).sh
benchmarks: $(bench_targets)
$(ceed.pc) : pkgconfig-prefix = $(abspath .)
$(OBJDIR)/ceed.pc : pkgconfig-prefix = $(prefix)
.INTERMEDIATE : $(OBJDIR)/ceed.pc
%/ceed.pc : ceed.pc.template | $$(@D)/.DIR
@$(SED) \
-e "s:%prefix%:$(pkgconfig-prefix):" \
-e "s:%libs_private%:$(pkgconfig-libs-private):" $< > $@
$(OBJDIR)/interface/ceed-jit-source-root-default.o : CPPFLAGS += -DCEED_JIT_SOURCE_ROOT_DEFAULT="\"$(abspath ./include)/\""
$(OBJDIR)/interface/ceed-jit-source-root-install.o : CPPFLAGS += -DCEED_JIT_SOURCE_ROOT_DEFAULT="\"$(abspath $(includedir))/\""
install : $(libceed) $(OBJDIR)/ceed.pc
$(INSTALL) -d $(addprefix $(if $(DESTDIR),"$(DESTDIR)"),"$(includedir)"\
"$(includedir)/ceed/" "$(includedir)/ceed/jit-source/"\
"$(includedir)/ceed/jit-source/cuda/" "$(includedir)/ceed/jit-source/hip/"\
"$(includedir)/ceed/jit-source/gallery/" "$(includedir)/ceed/jit-source/magma/"\
"$(includedir)/ceed/jit-source/sycl/" "$(libdir)" "$(pkgconfigdir)")
$(INSTALL_DATA) include/ceed/ceed.h "$(DESTDIR)$(includedir)/ceed/"
$(INSTALL_DATA) include/ceed/types.h "$(DESTDIR)$(includedir)/ceed/"
$(INSTALL_DATA) include/ceed/ceed-f32.h "$(DESTDIR)$(includedir)/ceed/"
$(INSTALL_DATA) include/ceed/ceed-f64.h "$(DESTDIR)$(includedir)/ceed/"
$(INSTALL_DATA) include/ceed/fortran.h "$(DESTDIR)$(includedir)/ceed/"
$(INSTALL_DATA) include/ceed/backend.h "$(DESTDIR)$(includedir)/ceed/"
$(INSTALL_DATA) include/ceed/cuda.h "$(DESTDIR)$(includedir)/ceed/"
$(INSTALL_DATA) include/ceed/hip.h "$(DESTDIR)$(includedir)/ceed/"
$(INSTALL_DATA) $(libceed) "$(DESTDIR)$(libdir)/"
$(INSTALL_DATA) $(OBJDIR)/ceed.pc "$(DESTDIR)$(pkgconfigdir)/"
$(INSTALL_DATA) include/ceed.h "$(DESTDIR)$(includedir)/"
$(INSTALL_DATA) include/ceedf.h "$(DESTDIR)$(includedir)/"
$(INSTALL_DATA) $(wildcard include/ceed/jit-source/cuda/*.h) "$(DESTDIR)$(includedir)/ceed/jit-source/cuda/"
$(INSTALL_DATA) $(wildcard include/ceed/jit-source/hip/*.h) "$(DESTDIR)$(includedir)/ceed/jit-source/hip/"
$(INSTALL_DATA) $(wildcard include/ceed/jit-source/gallery/*.h) "$(DESTDIR)$(includedir)/ceed/jit-source/gallery/"
$(INSTALL_DATA) $(wildcard include/ceed/jit-source/magma/*.h) "$(DESTDIR)$(includedir)/ceed/jit-source/magma/"
$(INSTALL_DATA) $(wildcard include/ceed/jit-source/sycl/*.h) "$(DESTDIR)$(includedir)/ceed/jit-source/sycl/"
.PHONY : all cln clean doxygen doc format lib install par print test tst prove prv prove-all junit examples tidy iwyu info info-backends info-backends-all
cln clean :
$(RM) -r $(OBJDIR) $(LIBDIR) dist *egg* .pytest_cache *cffi*
$(call quiet,MAKE) -C examples clean NEK5K_DIR="$(abspath $(NEK5K_DIR))"
$(call quiet,MAKE) -C python/tests clean
$(RM) benchmarks/*output.txt
distclean : clean
$(RM) -r doc/html doc/sphinx/build $(CONFIG)
DOXYGEN ?= doxygen
doxygen :
$(DOXYGEN) -q Doxyfile
doc-html doc-latexpdf doc-epub doc-livehtml : doc-% : doxygen
make -C doc/sphinx $*
doc : doc-html
CLANG_FORMAT ?= clang-format
CLANG_FORMAT_OPTS += -style=file -i
AUTOPEP8 ?= autopep8
AUTOPEP8_OPTS += --in-place --aggressive --max-line-length 120
format.ch := $(filter-out include/ceedf.h $(wildcard tests/t*-f.h), $(shell git ls-files '*.[ch]pp' '*.[ch]'))
format.py := $(filter-out tests/junit-xml/junit_xml/__init__.py, $(shell git ls-files '*.py'))
format-c :
$(CLANG_FORMAT) $(CLANG_FORMAT_OPTS) $(format.ch)
format-py :
$(AUTOPEP8) $(AUTOPEP8_OPTS) $(format.py)
format : format-c format-py
VERMIN ?= vermin
VERMIN_OPTS += -t=3.7- --violations
vermin :
$(VERMIN) $(VERMIN_OPTS) $(format.py)
CLANG_TIDY ?= clang-tidy
%.c.tidy : %.c
$(CLANG_TIDY) $(TIDY_OPTS) $^ -- $(CPPFLAGS) --std=c99 -I$(CUDA_DIR)/include -I$(ROCM_DIR)/include -DCEED_JIT_SOURCE_ROOT_DEFAULT="\"$(abspath ./include)/\""
%.cpp.tidy : %.cpp
$(CLANG_TIDY) $(TIDY_OPTS) $^ -- $(CPPFLAGS) --std=c++11 -I$(CUDA_DIR)/include -I$(OCCA_DIR)/include -I$(ROCM_DIR)/include
tidy-c : $(libceed.c:%=%.tidy)
tidy-cpp : $(libceed.cpp:%=%.tidy)
tidy : tidy-c tidy-cpp
ifneq ($(wildcard ../iwyu/*),)
IWYU_DIR ?= ../iwyu
IWYU_CC ?= $(IWYU_DIR)/build/bin/include-what-you-use
endif
iwyu :
$(MAKE) -B CC=$(IWYU_CC)
print :
@echo $(VAR)=$($(VAR))
print-% :
$(info [ variable name]: $*)
$(info [ origin]: $(origin $*))
$(info [ flavor]: $(flavor $*))
$(info [ value]: $(value $*))
$(info [expanded value]: $($*))
$(info )
@true
CONFIG_VARS = CC CXX FC NVCC NVCC_CXX HIPCC \
OPT CFLAGS CPPFLAGS CXXFLAGS FFLAGS NVCCFLAGS HIPCCFLAGS SYCLFLAGS \
AR ARFLAGS LDFLAGS LDLIBS LIBCXX SED \
MAGMA_DIR OCCA_DIR XSMM_DIR CUDA_DIR CUDA_ARCH MFEM_DIR PETSC_DIR NEK5K_DIR ROCM_DIR HIP_ARCH SYCL_DIR
needs_save = $(or $(filter command line,$(origin $(1))),$(filter simple,$(flavor $(1))))
configure :
$(file > $(CONFIG))
$(foreach v,$(CONFIG_VARS),$(if $(call needs_save,$(v)),$(file >> $(CONFIG),$(v) := $($(v)))))
@echo "Configuration cached in $(CONFIG):"
@cat $(CONFIG)
wheel : export MARCHFLAG = -march=generic
wheel : export WHEEL_PLAT = manylinux2010_x86_64
wheel :
docker run -it --user $(shell id -u):$(shell id -g) --rm -v $(PWD):/io -w /io \
-e MARCHFLAG -e WHEEL_PLAT \
quay.io/pypa/$(WHEEL_PLAT) python/make-wheels.sh
.PHONY : configure wheel
-include $(if $(filter B,$(MAKEFLAGS)),,$(libceed.c:%.c=$(OBJDIR)/%.d) $(tests.c:tests/%.c=$(OBJDIR)/%.d))