[Openmp-commits] [PATCH] D69859: [libomptarget] Replace forceinline with inline to work around nvcc deleting forceinline symbols

Jon Chesterfield via Phabricator via Openmp-commits openmp-commits at lists.llvm.org
Tue Nov 5 10:47:43 PST 2019


JonChesterfield created this revision.
JonChesterfield added reviewers: ABataev, jdoerfert, grokos, ikitayama, tianshilei1992.
Herald added a project: OpenMP.
Herald added a subscriber: openmp-commits.

[libomptarget] Replace forceinline with inline to work around nvcc deleting forceinline symbols

There is a problem with some installs of nvcc deleting the forceinline symbols from support.cu.
Adding the people who reported this as reviewers. This patch is an eductated guess at a fix,
posting it without a local repro for the failure. See D69857 <https://reviews.llvm.org/D69857> for an alternative.


Repository:
  rG LLVM Github Monorepo

https://reviews.llvm.org/D69859

Files:
  openmp/libomptarget/deviceRTLs/nvptx/src/target_impl.h


Index: openmp/libomptarget/deviceRTLs/nvptx/src/target_impl.h
===================================================================
--- openmp/libomptarget/deviceRTLs/nvptx/src/target_impl.h
+++ openmp/libomptarget/deviceRTLs/nvptx/src/target_impl.h
@@ -16,7 +16,7 @@
 #include "nvptx_interface.h"
 
 #define DEVICE __device__
-#define INLINE __forceinline__ DEVICE
+#define INLINE __inline__ DEVICE
 #define NOINLINE __noinline__ DEVICE
 
 ////////////////////////////////////////////////////////////////////////////////


-------------- next part --------------
A non-text attachment was scrubbed...
Name: D69859.227921.patch
Type: text/x-patch
Size: 520 bytes
Desc: not available
URL: <http://lists.llvm.org/pipermail/openmp-commits/attachments/20191105/2f38c302/attachment-0001.bin>


More information about the Openmp-commits mailing list