1# Copyright (c) 2017-2018, Lawrence Livermore National Security, LLC. 2# Produced at the Lawrence Livermore National Laboratory. LLNL-CODE-734707. 3# All Rights reserved. See files LICENSE and NOTICE for details. 4# 5# This file is part of CEED, a collection of benchmarks, miniapps, software 6# libraries and APIs for efficient high-order finite element and spectral 7# element discretizations for exascale applications. For more information and 8# source code availability see http://github.com/ceed. 9# 10# The CEED research is supported by the Exascale Computing Project 17-SC-20-SC, 11# a collaborative effort of two U.S. Department of Energy organizations (Office 12# of Science and the National Nuclear Security Administration) responsible for 13# the planning and preparation of a capable exascale ecosystem, including 14# software, applications, hardware, advanced system engineering and early 15# testbed platforms, in support of the nation's exascale computing imperative. 16 17CONFIG ?= config.mk 18-include $(CONFIG) 19COMMON ?= common.mk 20-include $(COMMON) 21 22ifeq (,$(filter-out undefined default,$(origin CC))) 23 CC = gcc 24endif 25ifeq (,$(filter-out undefined default,$(origin CXX))) 26 CXX = g++ 27endif 28ifeq (,$(filter-out undefined default,$(origin FC))) 29 FC = gfortran 30endif 31ifeq (,$(filter-out undefined default,$(origin LINK))) 32 LINK = $(CC) 33endif 34NVCC ?= $(CUDA_DIR)/bin/nvcc 35NVCC_CXX ?= $(CXX) 36HIPCC ?= $(HIP_DIR)/bin/hipcc 37 38# ASAN must be left empty if you don't want to use it 39ASAN ?= 40 41LDFLAGS ?= 42UNDERSCORE ?= 1 43 44# MFEM_DIR env variable should point to sibling directory 45ifneq ($(wildcard ../mfem/libmfem.*),) 46 MFEM_DIR ?= ../mfem 47endif 48 49# NEK5K_DIR env variable should point to sibling directory 50ifneq ($(wildcard ../Nek5000/*),) 51 NEK5K_DIR ?= $(abspath ../Nek5000) 52endif 53export NEK5K_DIR 54MPI ?= 1 55 56# CEED_DIR env for NEK5K testing 57export CEED_DIR = $(abspath .) 58 59# XSMM_DIR env variable should point to XSMM master (github.com/hfp/libxsmm) 60XSMM_DIR ?= ../libxsmm 61 62# OCCA_DIR env variable should point to OCCA master (github.com/libocca/occa) 63OCCA_DIR ?= ../occa 64 65# env variable MAGMA_DIR can be used too 66MAGMA_DIR ?= ../magma 67# If CUDA_DIR is not set, check for nvcc, or resort to /usr/local/cuda 68CUDA_DIR ?= $(or $(patsubst %/,%,$(dir $(patsubst %/,%,$(dir \ 69 $(shell which nvcc 2> /dev/null))))),/usr/local/cuda) 70HIP_DIR ?= /opt/rocm 71 72# Check for PETSc in ../petsc 73ifneq ($(wildcard ../petsc/lib/libpetsc.*),) 74 PETSC_DIR ?= ../petsc 75endif 76 77# Warning: SANTIZ options still don't run with /gpu/occa 78# export LSAN_OPTIONS=suppressions=.asanignore 79AFLAGS = -fsanitize=address #-fsanitize=undefined -fno-omit-frame-pointer 80 81CC_VENDOR := $(patsubst gcc%,gcc,$(firstword $(filter gcc% clang icc XL,$(shell $(CC) --version)))) 82FC_VENDOR := $(firstword $(filter GNU ifort XL,$(shell $(FC) --version 2>&1 || $(FC) -qversion))) 83 84# Default extra flags by vendor 85MARCHFLAG.gcc := -march=native 86MARCHFLAG.clang := $(MARCHFLAG.gcc) 87MARCHFLAG.icc := 88OMP_SIMD_FLAG.gcc := -fopenmp-simd 89OMP_SIMD_FLAG.clang := $(OMP_SIMD_FLAG.gcc) 90OMP_SIMD_FLAG.icc := -qopenmp-simd 91OPT.gcc := -ffp-contract=fast 92OPT.clang := $(OPT.gcc) 93CFLAGS.gcc := -fPIC -std=c99 -Wall -Wextra -Wno-unused-parameter -MMD -MP 94CFLAGS.clang := $(CFLAGS.gcc) 95CFLAGS.icc := $(CFLAGS.gcc) 96CFLAGS.XL := -qpic -MMD 97CXXFLAGS.gcc := -fPIC -std=c++11 -Wall -Wextra -Wno-unused-parameter -MMD -MP 98CXXFLAGS.clang := $(CXXFLAGS.gcc) 99CXXFLAGS.icc := $(CXXFLAGS.gcc) 100CXXFLAGS.XL := -qpic -MMD 101FFLAGS.GNU := -fPIC -cpp -Wall -Wextra -Wno-unused-parameter -Wno-unused-dummy-argument -MMD -MP 102FFLAGS.ifort := -fPIC -cpp 103FFLAGS.XL := -qpic -ffree-form -qpreprocess -qextname -MMD 104 105# This check works with compilers that use gcc and clang. It fails with some 106# compilers; e.g., xlc apparently ignores all options when -E is passed, thus 107# succeeds with any flags. Users can pass MARCHFLAG=... if desired. 108cc_check_flag = $(shell $(CC) -E -Werror $(1) -x c /dev/null > /dev/null 2>&1 && echo 1) 109MARCHFLAG := $(MARCHFLAG.$(CC_VENDOR)) 110MARCHFLAG := $(if $(call cc_check_flag,$(MARCHFLAG)),$(MARCHFLAG),-mcpu=native) 111MARCHFLAG := $(if $(call cc_check_flag,$(MARCHFLAG)),$(MARCHFLAG)) 112 113OMP_SIMD_FLAG := $(OMP_SIMD_FLAG.$(CC_VENDOR)) 114OMP_SIMD_FLAG := $(if $(call cc_check_flag,$(OMP_SIMD_FLAG)),$(OMP_SIMD_FLAG)) 115 116OPT ?= -O -g $(MARCHFLAG) $(OPT.$(CC_VENDOR)) $(OMP_SIMD_FLAG) 117CFLAGS ?= $(OPT) $(CFLAGS.$(CC_VENDOR)) 118CXXFLAGS ?= $(OPT) $(CXXFLAGS.$(CC_VENDOR)) 119NVCCFLAGS ?= -ccbin $(CXX) -Xcompiler "$(OPT)" -Xcompiler -fPIC 120HIPCCFLAGS ?= $(OPT) -fPIC 121FFLAGS ?= $(OPT) $(FFLAGS.$(FC_VENDOR)) 122 123ifeq ($(COVERAGE), 1) 124 CFLAGS += --coverage 125 LDFLAGS += --coverage 126endif 127 128CFLAGS += $(if $(ASAN),$(AFLAGS)) 129FFLAGS += $(if $(ASAN),$(AFLAGS)) 130LDFLAGS += $(if $(ASAN),$(AFLAGS)) 131CPPFLAGS += -I./include 132LDLIBS = -lm 133OBJDIR := build 134LIBDIR := lib 135 136# Installation variables 137prefix ?= /usr/local 138bindir = $(prefix)/bin 139libdir = $(prefix)/lib 140includedir = $(prefix)/include 141pkgconfigdir = $(libdir)/pkgconfig 142INSTALL = install 143INSTALL_PROGRAM = $(INSTALL) 144INSTALL_DATA = $(INSTALL) -m644 145 146# Get number of processors of the machine 147NPROCS := $(shell getconf _NPROCESSORS_ONLN) 148# prepare make options to run in parallel 149MFLAGS := -j $(NPROCS) --warn-undefined-variables \ 150 --no-print-directory --no-keep-going 151 152PYTHON ?= python3 153PROVE ?= prove 154PROVE_OPTS ?= -j $(NPROCS) 155DARWIN := $(filter Darwin,$(shell uname -s)) 156SO_EXT := $(if $(DARWIN),dylib,so) 157 158ceed.pc := $(LIBDIR)/pkgconfig/ceed.pc 159libceed := $(LIBDIR)/libceed.$(SO_EXT) 160CEED_LIBS = -lceed 161libceed.c := $(wildcard interface/ceed*.c) 162gallery.c := $(wildcard gallery/*/ceed*.c) 163libceed.c += $(gallery.c) 164libceed_test := $(LIBDIR)/libceed_test.$(SO_EXT) 165libceeds = $(libceed) $(libceed_test) 166BACKENDS_BUILTIN := /cpu/self/ref/serial /cpu/self/ref/blocked /cpu/self/opt/serial /cpu/self/opt/blocked 167BACKENDS := $(BACKENDS_BUILTIN) 168 169# Tests 170tests.c := $(sort $(wildcard tests/t[0-9][0-9][0-9]-*.c)) 171tests.f := $(sort $(wildcard tests/t[0-9][0-9][0-9]-*.f90)) 172tests := $(tests.c:tests/%.c=$(OBJDIR)/%) 173ctests := $(tests) 174tests += $(tests.f:tests/%.f90=$(OBJDIR)/%) 175# Examples 176examples.c := $(sort $(wildcard examples/ceed/*.c)) 177examples.f := $(sort $(wildcard examples/ceed/*.f)) 178examples := $(examples.c:examples/ceed/%.c=$(OBJDIR)/%) 179examples += $(examples.f:examples/ceed/%.f=$(OBJDIR)/%) 180# MFEM Examples 181mfemexamples.cpp := $(sort $(wildcard examples/mfem/*.cpp)) 182mfemexamples := $(mfemexamples.cpp:examples/mfem/%.cpp=$(OBJDIR)/mfem-%) 183# Nek5K Examples 184nekexamples := $(OBJDIR)/nek-bps 185# PETSc Examples 186petscexamples.c := $(wildcard examples/petsc/*.c) 187petscexamples := $(petscexamples.c:examples/petsc/%.c=$(OBJDIR)/petsc-%) 188# Fluid Dynamics Examples 189fluidsexamples.c := $(sort $(wildcard examples/fluids/*.c)) 190fluidsexamples := $(fluidsexamples.c:examples/fluids/%.c=$(OBJDIR)/fluids-%) 191# Solid Mechanics Examples 192solidsexamples.c := $(sort $(wildcard examples/solids/*.c)) 193solidsexamples := $(solidsexamples.c:examples/solids/%.c=$(OBJDIR)/solids-%) 194 195# Backends/[ref, blocked, template, memcheck, opt, avx, occa, magma] 196ref.c := $(sort $(wildcard backends/ref/*.c)) 197blocked.c := $(sort $(wildcard backends/blocked/*.c)) 198template.c := $(sort $(wildcard backends/template/*.c)) 199ceedmemcheck.c := $(sort $(wildcard backends/memcheck/*.c)) 200opt.c := $(sort $(wildcard backends/opt/*.c)) 201avx.c := $(sort $(wildcard backends/avx/*.c)) 202xsmm.c := $(sort $(wildcard backends/xsmm/*.c)) 203cuda.c := $(sort $(wildcard backends/cuda/*.c)) 204cuda.cpp := $(sort $(wildcard backends/cuda/*.cpp)) 205cuda.cu := $(sort $(wildcard backends/cuda/kernels/*.cu)) 206cuda-reg.c := $(sort $(wildcard backends/cuda-reg/*.c)) 207cuda-reg.cu := $(sort $(wildcard backends/cuda-reg/kernels/*.cu)) 208cuda-shared.c := $(sort $(wildcard backends/cuda-shared/*.c)) 209cuda-shared.cu := $(sort $(wildcard backends/cuda-shared/kernels/*.cu)) 210cuda-gen.c := $(sort $(wildcard backends/cuda-gen/*.c)) 211cuda-gen.cpp := $(sort $(wildcard backends/cuda-gen/*.cpp)) 212cuda-gen.cu := $(sort $(wildcard backends/cuda-gen/kernels/*.cu)) 213occa.cpp := $(sort $(shell find backends/occa -type f -name *.cpp)) 214magma.c := $(sort $(wildcard backends/magma/*.c)) 215magma.cu := $(sort $(wildcard backends/magma/kernels/cuda/*.cu)) 216magma.hip := $(sort $(wildcard backends/magma/kernels/hip/*.hip.cpp)) 217hip.c := $(sort $(wildcard backends/hip/*.c)) 218hip.cpp := $(sort $(wildcard backends/hip/*.cpp)) 219hip.hip := $(sort $(wildcard backends/hip/kernels/*.hip.cpp)) 220 221# Quiet, color output 222quiet ?= $($(1)) 223 224# Cancel built-in and old-fashioned implicit rules which we don't use 225.SUFFIXES: 226 227.SECONDEXPANSION: # to expand $$(@D)/.DIR 228 229%/.DIR : 230 @mkdir -p $(@D) 231 @touch $@ 232 233.PRECIOUS: %/.DIR 234 235lib: $(libceed) $(ceed.pc) 236# run 'lib' target in parallel 237par:;@$(MAKE) $(MFLAGS) V=$(V) lib 238backend_status = $(if $(filter $1,$(BACKENDS)), [backends: $1], [not found]) 239info: 240 $(info ------------------------------------) 241 $(info CC = $(CC)) 242 $(info CXX = $(CXX)) 243 $(info FC = $(FC)) 244 $(info CPPFLAGS = $(CPPFLAGS)) 245 $(info CFLAGS = $(value CFLAGS)) 246 $(info CXXFLAGS = $(value CXXFLAGS)) 247 $(info FFLAGS = $(value FFLAGS)) 248 $(info NVCCFLAGS = $(value NVCCFLAGS)) 249 $(info HIPCCFLAGS = $(value HIPCCFLAGS)) 250 $(info LDFLAGS = $(value LDFLAGS)) 251 $(info LDLIBS = $(LDLIBS)) 252 $(info OPT = $(OPT)) 253 $(info AFLAGS = $(AFLAGS)) 254 $(info ASAN = $(or $(ASAN),(empty))) 255 $(info V = $(or $(V),(empty)) [verbose=$(if $(V),on,off)]) 256 $(info ------------------------------------) 257 $(info MEMCHK_STATUS = $(MEMCHK_STATUS)$(call backend_status,/cpu/self/memcheck/serial /cpu/sef/memcheck/blocked)) 258 $(info AVX_STATUS = $(AVX_STATUS)$(call backend_status,/cpu/self/avx/serial /cpu/self/avx/blocked)) 259 $(info XSMM_DIR = $(XSMM_DIR)$(call backend_status,/cpu/self/xsmm/serial /cpu/self/xsmm/blocked)) 260 $(info OCCA_DIR = $(OCCA_DIR)$(call backend_status,$(OCCA_BACKENDS))) 261 $(info MAGMA_DIR = $(MAGMA_DIR)$(call backend_status,/gpu/magma /gpu/magma/det)) 262 $(info CUDA_DIR = $(CUDA_DIR)$(call backend_status,$(CUDA_BACKENDS))) 263 $(info HIP_DIR = $(HIP_DIR)$(call backend_status,$(HIP_BACKENDS))) 264 $(info ------------------------------------) 265 $(info MFEM_DIR = $(MFEM_DIR)) 266 $(info NEK5K_DIR = $(NEK5K_DIR)) 267 $(info PETSC_DIR = $(PETSC_DIR)) 268 $(info ------------------------------------) 269 $(info prefix = $(prefix)) 270 $(info includedir = $(value includedir)) 271 $(info libdir = $(value libdir)) 272 $(info pkgconfigdir = $(value pkgconfigdir)) 273 $(info ------------------------------------) 274 @true 275info-backends: 276 $(info make: 'lib' with optional backends: $(filter-out $(BACKENDS_BUILTIN),$(BACKENDS))) 277.PHONY: lib all par info info-backends 278 279$(libceed) : LDFLAGS += $(if $(DARWIN), -install_name @rpath/$(notdir $(libceed))) 280$(libceed_test) : LDFLAGS += $(if $(DARWIN), -install_name @rpath/$(notdir $(libceed_test))) 281 282# Standard Backends 283libceed.c += $(ref.c) 284libceed.c += $(blocked.c) 285libceed.c += $(opt.c) 286 287# Testing Backends 288test_backends.c := $(template.c) 289TEST_BACKENDS := /cpu/self/tmpl /cpu/self/tmpl/sub 290 291# Memcheck Backend 292MEMCHK_STATUS = Disabled 293MEMCHK := $(shell echo "\#include <valgrind/memcheck.h>" | $(CC) $(CPPFLAGS) -E - >/dev/null 2>&1 && echo 1) 294ifeq ($(MEMCHK),1) 295 MEMCHK_STATUS = Enabled 296 libceed.c += $(ceedmemcheck.c) 297 BACKENDS += /cpu/self/memcheck/serial /cpu/self/memcheck/blocked 298endif 299 300# AVX Backed 301AVX_STATUS = Disabled 302AVX_FLAG := $(if $(filter clang,$(CC_VENDOR)),+avx,-mavx) 303AVX := $(filter $(AVX_FLAG),$(shell $(CC) $(OPT) -v -E -x c /dev/null 2>&1)) 304ifneq ($(AVX),) 305 AVX_STATUS = Enabled 306 libceed.c += $(avx.c) 307 BACKENDS += /cpu/self/avx/serial /cpu/self/avx/blocked 308endif 309 310# libXSMM Backends 311ifneq ($(wildcard $(XSMM_DIR)/lib/libxsmm.*),) 312 $(libceeds) : LDFLAGS += -L$(XSMM_DIR)/lib -Wl,-rpath,$(abspath $(XSMM_DIR)/lib) 313 $(libceeds) : LDLIBS += -lxsmm -ldl 314 MKL ?= 315 ifeq (,$(MKL)$(MKLROOT)) 316 BLAS_LIB = -lblas 317 else 318 ifneq ($(MKLROOT),) 319 # Some installs put everything inside an intel64 subdirectory, others not 320 MKL_LIBDIR = $(dir $(firstword $(wildcard $(MKLROOT)/lib/intel64/libmkl_sequential.* $(MKLROOT)/lib/libmkl_sequential.*))) 321 MKL_LINK = -L$(MKL_LIBDIR) -Wl,-rpath,$(MKL_LIBDIR) 322 endif 323 BLAS_LIB = $(MKL_LINK) -Wl,--no-as-needed -lmkl_intel_lp64 -lmkl_sequential -lmkl_core -lpthread -lm -ldl 324 endif 325 $(libceeds) : LDLIBS += $(BLAS_LIB) 326 libceed.c += $(xsmm.c) 327 $(xsmm.c:%.c=$(OBJDIR)/%.o) $(xsmm.c:%=%.tidy) : CPPFLAGS += -I$(XSMM_DIR)/include 328 BACKENDS += /cpu/self/xsmm/serial /cpu/self/xsmm/blocked 329endif 330 331# OCCA Backends 332OCCA_BACKENDS = /cpu/occa/serial 333ifneq ($(wildcard $(OCCA_DIR)/lib/libocca.*),) 334 OCCA_MODES := $(shell $(OCCA_DIR)/bin/occa modes) 335 OCCA_BACKENDS += $(if $(filter OpenMP,$(OCCA_MODES)),/cpu/occa/openmp) 336# OCCA_BACKENDS += $(if $(filter OpenCL,$(OCCA_MODES)),/opencl/occa) 337 OCCA_BACKENDS += $(if $(filter HIP,$(OCCA_MODES)),/gpu/occa/hip) 338 OCCA_BACKENDS += $(if $(filter CUDA,$(OCCA_MODES)),/gpu/occa/cuda) 339 340 $(libceeds) : CPPFLAGS += -I$(OCCA_DIR)/include 341 $(libceeds) : LDFLAGS += -L$(OCCA_DIR)/lib -Wl,-rpath,$(abspath $(OCCA_DIR)/lib) 342 $(libceeds) : LDLIBS += -locca 343 $(libceeds) : LINK = $(CXX) 344 libceed.cpp += $(occa.cpp) 345 BACKENDS += $(OCCA_BACKENDS) 346endif 347 348# CUDA Backends 349CUDA_LIB_DIR := $(wildcard $(foreach d,lib lib64,$(CUDA_DIR)/$d/libcudart.${SO_EXT})) 350CUDA_LIB_DIR := $(patsubst %/,%,$(dir $(firstword $(CUDA_LIB_DIR)))) 351CUDA_LIB_DIR_STUBS := $(CUDA_LIB_DIR)/stubs 352CUDA_BACKENDS = /gpu/cuda/ref /gpu/cuda/reg /gpu/cuda/shared /gpu/cuda/gen 353ifneq ($(CUDA_LIB_DIR),) 354 $(libceeds) : CPPFLAGS += -I$(CUDA_DIR)/include 355 $(libceeds) : LDFLAGS += -L$(CUDA_LIB_DIR) -Wl,-rpath,$(abspath $(CUDA_LIB_DIR)) 356 $(libceeds) : LDLIBS += -lcudart -lnvrtc -lcuda -lcublas 357 $(libceeds) : LINK = $(CXX) 358 libceed.c += $(cuda.c) $(cuda-reg.c) $(cuda-shared.c) $(cuda-gen.c) 359 libceed.cpp += $(cuda.cpp) $(cuda-gen.cpp) 360 libceed.cu += $(cuda.cu) $(cuda-reg.cu) $(cuda-shared.cu) $(cuda-gen.cu) 361 BACKENDS += $(CUDA_BACKENDS) 362endif 363 364# HIP Backends 365HIP_LIB_DIR := $(wildcard $(foreach d,lib lib64,$(HIP_DIR)/$d/libamdhip64.${SO_EXT})) 366HIP_LIB_DIR := $(patsubst %/,%,$(dir $(firstword $(HIP_LIB_DIR)))) 367HIP_BACKENDS = /gpu/hip/ref 368ifneq ($(HIP_LIB_DIR),) 369 $(libceeds) : HIPCCFLAGS += -I./include 370 ifneq ($(CXX), $(HIPCC)) 371 CPPFLAGS += $(subst =,,$(shell $(HIP_DIR)/bin/hipconfig -C)) 372 endif 373 CPPFLAGS += -I$(HIP_DIR)/include -Wno-unused-function 374 $(libceeds) : LDFLAGS += -L$(HIP_LIB_DIR) -Wl,-rpath,$(abspath $(HIP_LIB_DIR)) 375 $(libceeds) : LDLIBS += -lamdhip64 -lhipblas 376 $(libceeds) : LINK = $(CXX) 377 libceed.hip += $(hip.hip) 378 libceed.cpp += $(hip.cpp) 379 libceed.c += $(hip.c) 380 BACKENDS += $(HIP_BACKENDS) 381endif 382 383# MAGMA Backend 384ifneq ($(wildcard $(MAGMA_DIR)/lib/libmagma.*),) 385 ifneq ($(CUDA_LIB_DIR),) 386 cuda_link = -Wl,-rpath,$(CUDA_LIB_DIR) -L$(CUDA_LIB_DIR) -lcublas -lcusparse -lcudart 387 omp_link = -fopenmp 388 magma_link_static = -L$(MAGMA_DIR)/lib -lmagma $(cuda_link) $(omp_link) 389 magma_link_shared = -L$(MAGMA_DIR)/lib -Wl,-rpath,$(abspath $(MAGMA_DIR)/lib) -lmagma 390 magma_link := $(if $(wildcard $(MAGMA_DIR)/lib/libmagma.${SO_EXT}),$(magma_link_shared),$(magma_link_static)) 391 $(libceeds) : LDLIBS += $(magma_link) 392 $(tests) $(examples) : LDLIBS += $(magma_link) 393 libceed.c += $(magma.c) 394 libceed.cu += $(magma.cu) 395 $(magma.c:%.c=$(OBJDIR)/%.o) $(magma.c:%=%.tidy) : CPPFLAGS += -DADD_ -I$(MAGMA_DIR)/include -I$(CUDA_DIR)/include 396 $(magma.cu:%.cu=$(OBJDIR)/%.o) : CPPFLAGS += --compiler-options=-fPIC -DADD_ -I$(MAGMA_DIR)/include -I$(MAGMA_DIR)/magmablas -I$(MAGMA_DIR)/control -I$(CUDA_DIR)/include 397 BACKENDS += /gpu/magma /gpu/magma/det 398 else 399 ifneq ($(HIP_LIB_DIR),) 400 hip_link = -Wl,-rpath,$(HIP_LIB_DIR) -L$(HIP_LIB_DIR) -lhipblas -lhipsparse -lamdhip64 401 omp_link = -fopenmp 402 magma_link_static = -L$(MAGMA_DIR)/lib -lmagma $(hip_link) $(omp_link) 403 magma_link_shared = -L$(MAGMA_DIR)/lib -Wl,-rpath,$(abspath $(MAGMA_DIR)/lib) -lmagma 404 magma_link := $(if $(wildcard $(MAGMA_DIR)/lib/libmagma.${SO_EXT}),$(magma_link_shared),$(magma_link_static)) 405 $(libceeds) : LDLIBS += $(magma_link) 406 $(tests) $(examples) : LDLIBS += $(magma_link) 407 libceed.c += $(magma.c) 408 libceed.hip += $(magma.hip) 409 ifneq ($(CXX), $(HIPCC)) 410 $(magma.c:%.c=$(OBJDIR)/%.o) $(magma.c:%=%.tidy) : CPPFLAGS += -I$(MAGMA_DIR)/include -I$(HIP_DIR)/include -DHAVE_HIP -DADD_ 411 else 412 $(magma.c:%.c=$(OBJDIR)/%.o) $(magma.c:%=%.tidy) : HIPCCFLAGS += -I$(MAGMA_DIR)/include -I$(HIP_DIR)/include -DHAVE_HIP -DADD_ 413 endif 414 $(magma.hip:%.hip.cpp=$(OBJDIR)/%.o) : HIPCCFLAGS += -I$(MAGMA_DIR)/include -I$(MAGMA_DIR)/magmablas -I$(MAGMA_DIR)/control -I$(HIP_DIR)/include -DHAVE_HIP -DADD_ 415 BACKENDS += /gpu/magma 416 endif 417 endif 418endif 419 420export BACKENDS 421 422libceed.o = $(libceed.c:%.c=$(OBJDIR)/%.o) $(libceed.cpp:%.cpp=$(OBJDIR)/%.o) $(libceed.cu:%.cu=$(OBJDIR)/%.o) $(libceed.hip:%.hip.cpp=$(OBJDIR)/%.o) 423$(filter %fortran.o,$(libceed.o)) : CPPFLAGS += $(if $(filter 1,$(UNDERSCORE)),-DUNDERSCORE) 424$(libceed.o): | info-backends 425$(libceed) : $(libceed.o) | $$(@D)/.DIR 426 $(call quiet,LINK) $(LDFLAGS) -shared -o $@ $^ $(LDLIBS) 427 428$(OBJDIR)/%.o : $(CURDIR)/%.c | $$(@D)/.DIR 429 $(call quiet,CC) $(CPPFLAGS) $(CFLAGS) -c -o $@ $(abspath $<) 430 431$(OBJDIR)/%.o : $(CURDIR)/%.cpp | $$(@D)/.DIR 432 $(call quiet,CXX) $(CPPFLAGS) $(CXXFLAGS) -c -o $@ $(abspath $<) 433 434$(OBJDIR)/%.o : $(CURDIR)/%.cu | $$(@D)/.DIR 435 $(call quiet,NVCC) $(filter-out -Wno-unused-function, $(CPPFLAGS)) $(NVCCFLAGS) -c -o $@ $(abspath $<) 436 437$(OBJDIR)/%.o : $(CURDIR)/%.hip.cpp | $$(@D)/.DIR 438 $(call quiet,HIPCC) $(HIPCCFLAGS) -c -o $@ $(abspath $<) 439 440$(OBJDIR)/% : tests/%.c | $$(@D)/.DIR 441 $(call quiet,LINK.c) $(CEED_LDFLAGS) -o $@ $(abspath $<) $(CEED_LIBS) $(LDLIBS) 442 443$(OBJDIR)/% : tests/%.f90 | $$(@D)/.DIR 444 $(call quiet,LINK.F) -DSOURCE_DIR='"$(abspath $(<D))/"' $(CEED_LDFLAGS) -o $@ $(abspath $<) $(CEED_LIBS) $(LDLIBS) 445 446$(OBJDIR)/% : examples/ceed/%.c | $$(@D)/.DIR 447 $(call quiet,LINK.c) $(CEED_LDFLAGS) -o $@ $(abspath $<) $(CEED_LIBS) $(LDLIBS) 448 449$(OBJDIR)/% : examples/ceed/%.f | $$(@D)/.DIR 450 $(call quiet,LINK.F) -DSOURCE_DIR='"$(abspath $(<D))/"' $(CEED_LDFLAGS) -o $@ $(abspath $<) $(CEED_LIBS) $(LDLIBS) 451 452$(OBJDIR)/mfem-% : examples/mfem/%.cpp $(libceed) | $$(@D)/.DIR 453 +$(MAKE) -C examples/mfem CEED_DIR=`pwd` \ 454 MFEM_DIR="$(abspath $(MFEM_DIR))" CXX=$(CXX) $* 455 mv examples/mfem/$* $@ 456 457# Note: Multiple Nek files cannot be built in parallel. The '+' here enables 458# this single Nek bps file to be built in parallel with other examples, 459# such as when calling `make prove-all -j2`. 460$(OBJDIR)/nek-bps : examples/nek/bps/bps.usr examples/nek/nek-examples.sh $(libceed) | $$(@D)/.DIR 461 +$(MAKE) -C examples MPI=$(MPI) CEED_DIR=`pwd` NEK5K_DIR="$(abspath $(NEK5K_DIR))" nek 462 mv examples/nek/build/bps $(OBJDIR)/bps 463 cp examples/nek/nek-examples.sh $(OBJDIR)/nek-bps 464 465$(OBJDIR)/petsc-% : examples/petsc/%.c $(libceed) $(ceed.pc) | $$(@D)/.DIR 466 +$(MAKE) -C examples/petsc CEED_DIR=`pwd` \ 467 PETSC_DIR="$(abspath $(PETSC_DIR))" OPT="$(OPT)" $* 468 mv examples/petsc/$* $@ 469 470$(OBJDIR)/fluids-% : examples/fluids/%.c $(libceed) $(ceed.pc) | $$(@D)/.DIR 471 +$(MAKE) -C examples/fluids CEED_DIR=`pwd` \ 472 PETSC_DIR="$(abspath $(PETSC_DIR))" OPT="$(OPT)" $* 473 mv examples/fluids/$* $@ 474 475$(OBJDIR)/solids-% : examples/solids/%.c $(libceed) $(ceed.pc) | $$(@D)/.DIR 476 +$(MAKE) -C examples/solids CEED_DIR=`pwd` \ 477 PETSC_DIR="$(abspath $(PETSC_DIR))" OPT="$(OPT)" $* 478 mv examples/solids/$* $@ 479 480libceed_test.o = $(test_backends.c:%.c=$(OBJDIR)/%.o) 481$(libceed_test) : $(libceed.o) $(libceed_test.o) | $$(@D)/.DIR 482 $(call quiet,LINK) $(LDFLAGS) -shared -o $@ $^ $(LDLIBS) 483 484$(examples) : $(libceed) 485$(tests) : $(libceed_test) 486$(tests) : CEED_LIBS = -lceed_test 487$(tests) $(examples) : LDFLAGS += -Wl,-rpath,$(abspath $(LIBDIR)) -L$(LIBDIR) 488 489run-t% : BACKENDS += $(TEST_BACKENDS) 490run-% : $(OBJDIR)/% 491 @tests/tap.sh $(<:$(OBJDIR)/%=%) 492 493external_examples := \ 494 $(if $(MFEM_DIR),$(mfemexamples)) \ 495 $(if $(PETSC_DIR),$(petscexamples)) \ 496 $(if $(NEK5K_DIR),$(nekexamples)) \ 497 $(if $(PETSC_DIR),$(fluidsexamples)) \ 498 $(if $(PETSC_DIR),$(solidsexamples)) 499 500allexamples = $(examples) $(external_examples) 501 502# The test and prove targets can be controlled via pattern searches. The 503# default is to run tests and those examples that have no external dependencies. 504# Examples of finer grained control: 505# 506# make test search='petsc mfem' # PETSc and MFEM examples 507# make prove search='t3' # t3xx series tests 508# make junit search='ex petsc' # core ex* and PETSc tests 509search ?= t ex 510realsearch = $(search:%=%%) 511matched = $(foreach pattern,$(realsearch),$(filter $(OBJDIR)/$(pattern),$(tests) $(allexamples))) 512 513# Test core libCEED 514test : $(matched:$(OBJDIR)/%=run-%) 515 516# Run test target in parallel 517tst : ;@$(MAKE) $(MFLAGS) V=$(V) test 518# CPU C tests only for backend % 519ctc-% : $(ctests);@$(foreach tst,$(ctests),$(tst) /cpu/$*;) 520 521prove : BACKENDS += $(TEST_BACKENDS) 522prove : $(matched) 523 $(info Testing backends: $(BACKENDS)) 524 $(PROVE) $(PROVE_OPTS) --exec 'tests/tap.sh' $(matched:$(OBJDIR)/%=%) 525# Run prove target in parallel 526prv : ;@$(MAKE) $(MFLAGS) V=$(V) prove 527 528prove-all : 529 +$(MAKE) prove realsearch=% 530 531junit-t% : BACKENDS += $(TEST_BACKENDS) 532junit-% : $(OBJDIR)/% 533 @printf " %10s %s\n" TEST $(<:$(OBJDIR)/%=%); $(PYTHON) tests/junit.py $(<:$(OBJDIR)/%=%) 534 535junit : $(matched:$(OBJDIR)/%=junit-%) 536 537all: $(alltests) 538 539examples : $(allexamples) 540ceedexamples : $(examples) 541nekexamples : $(nekexamples) 542mfemexamples : $(mfemexamples) 543petscexamples : $(petscexamples) 544 545# Benchmarks 546allbenchmarks = petsc-bps 547bench_targets = $(addprefix bench-,$(allbenchmarks)) 548.PHONY: $(bench_targets) benchmarks 549$(bench_targets): bench-%: $(OBJDIR)/% 550 cd benchmarks && ./benchmark.sh --ceed "$(BACKENDS)" -r $(*).sh 551benchmarks: $(bench_targets) 552 553$(ceed.pc) : pkgconfig-prefix = $(abspath .) 554$(OBJDIR)/ceed.pc : pkgconfig-prefix = $(prefix) 555.INTERMEDIATE : $(OBJDIR)/ceed.pc 556%/ceed.pc : ceed.pc.template | $$(@D)/.DIR 557 @sed "s:%prefix%:$(pkgconfig-prefix):" $< > $@ 558 559install : $(libceed) $(OBJDIR)/ceed.pc 560 $(INSTALL) -d $(addprefix $(if $(DESTDIR),"$(DESTDIR)"),"$(includedir)"\ 561 "$(libdir)" "$(pkgconfigdir)") 562 $(INSTALL_DATA) include/ceed.h "$(DESTDIR)$(includedir)/" 563 $(INSTALL_DATA) include/ceedf.h "$(DESTDIR)$(includedir)/" 564 $(INSTALL_DATA) $(libceed) "$(DESTDIR)$(libdir)/" 565 $(INSTALL_DATA) $(OBJDIR)/ceed.pc "$(DESTDIR)$(pkgconfigdir)/" 566 567.PHONY : cln clean doxygen doc lib install all print test tst prove prv prove-all junit examples style style-c style-py tidy info info-backends 568 569cln clean : 570 $(RM) -r $(OBJDIR) $(LIBDIR) dist *egg* .pytest_cache *cffi* 571 $(MAKE) -C examples clean NEK5K_DIR="$(abspath $(NEK5K_DIR))" 572 $(MAKE) -C tests/python clean 573 $(RM) benchmarks/*output.txt 574 575distclean : clean 576 $(RM) -r doc/html doc/sphinx/build $(CONFIG) 577 578DOXYGEN ?= doxygen 579doxygen : 580 $(DOXYGEN) Doxyfile 581 582doc-html doc-latexpdf doc-epub : doc-% : doxygen 583 make -C doc/sphinx $* 584 585doc : doc-html 586 587style-c : 588 @astyle --options=.astylerc \ 589 $(filter-out include/ceedf.h $(wildcard tests/t*-f.h), \ 590 $(wildcard include/*.h interface/*.[ch] tests/*.[ch] backends/*/*.[ch] \ 591 examples/*/*/*.[ch] examples/*/*.[ch] examples/*/*.[ch]pp gallery/*/*.[ch])) 592 593AUTOPEP8 = autopep8 594style-py : AUTOPEP8_ARGS = --in-place --aggressive 595style-py : 596 @$(AUTOPEP8) $(AUTOPEP8_ARGS) $(wildcard *.py python**/*.py tests/python**/*.py examples**/*.py doc/sphinx/source**/*.py benchmarks/*.py) 597 598style : style-c style-py 599 600CLANG_TIDY ?= clang-tidy 601 602%.c.tidy : %.c 603 $(CLANG_TIDY) $(TIDY_OPTS) $^ -- $(CPPFLAGS) --std=c99 -I$(CUDA_DIR)/include 604 605%.cpp.tidy : %.cpp 606 $(CLANG_TIDY) $(TIDY_OPTS) $^ -- $(CPPFLAGS) --std=c++11 -I$(CUDA_DIR)/include -I$(OCCA_DIR)/include 607 608tidy_c : $(libceed.c:%=%.tidy) 609tidy_cpp : $(libceed.cpp:%=%.tidy) 610 611tidy : tidy_c tidy_cpp 612 613print : 614 @echo $(VAR)=$($(VAR)) 615 616print-% : 617 $(info [ variable name]: $*) 618 $(info [ origin]: $(origin $*)) 619 $(info [ flavor]: $(flavor $*)) 620 $(info [ value]: $(value $*)) 621 $(info [expanded value]: $($*)) 622 $(info ) 623 @true 624 625# "make configure" detects any variables passed on the command line or 626# previously set in config.mk, caching them in config.mk as simple 627# (:=) variables. Variables set in config.mk or on the command line 628# take precedence over the defaults provided in the file. Typical 629# usage: 630# 631# make configure CC=/path/to/my/cc CUDA_DIR=/opt/cuda 632# make 633# make prove 634# 635# The values in the file can be updated by passing them on the command 636# line, e.g., 637# 638# make configure CC=/path/to/other/clang 639 640# All variables to consider for caching 641CONFIG_VARS = CC CXX FC NVCC NVCC_CXX HIPCC \ 642 OPT CFLAGS CPPFLAGS CXXFLAGS FFLAGS NVCCFLAGS HIPCCFLAGS \ 643 LDFLAGS LDLIBS \ 644 MAGMA_DIR XSMM_DIR CUDA_DIR MFEM_DIR PETSC_DIR NEK5K_DIR HIP_DIR 645 646# $(call needs_save,CFLAGS) returns true (a nonempty string) if CFLAGS 647# was set on the command line or in config.mk (where it will appear as 648# a simple variable). 649needs_save = $(or $(filter command line,$(origin $(1))),$(filter simple,$(flavor $(1)))) 650 651configure : 652 $(file > $(CONFIG)) 653 $(foreach v,$(CONFIG_VARS),$(if $(call needs_save,$(v)),$(file >> $(CONFIG),$(v) := $($(v))))) 654 @echo "Configuration cached in $(CONFIG):" 655 @cat $(CONFIG) 656 657wheel : export MARCHFLAG = -march=generic 658wheel : export WHEEL_PLAT = manylinux2010_x86_64 659wheel : 660 docker run -it --user $(shell id -u):$(shell id -g) --rm -v $(PWD):/io -w /io \ 661 -e MARCHFLAG -e WHEEL_PLAT \ 662 quay.io/pypa/$(WHEEL_PLAT) python/make-wheels.sh 663 664.PHONY : configure wheel 665 666# Include *.d deps when not -B = --always-make: useful if the paths are wonky in a container 667-include $(if $(filter B,$(MAKEFLAGS)),,$(libceed.c:%.c=$(OBJDIR)/%.d) $(tests.c:tests/%.c=$(OBJDIR)/%.d)) 668