* [ITA] pocl
@ 2024-01-03 5:14 Takashi Yano
2024-01-03 5:25 ` Takashi Yano
0 siblings, 1 reply; 18+ messages in thread
From: Takashi Yano @ 2024-01-03 5:14 UTC (permalink / raw)
To: cygwin-apps
[-- Attachment #1: Type: text/plain, Size: 142 bytes --]
I'd like to adopt the pocl package.
- Update to latest upstream release.
- Enable CUDA support.
--
Takashi Yano <takashi.yano@nifty.ne.jp>
[-- Attachment #2: pocl.cygport --]
[-- Type: text/plain, Size: 1763 bytes --]
inherit clang cmake
NAME="pocl"
VERSION=3.1
RELEASE=1
CATEGORY="Libs"
# The entire code is under MIT
# include/utlist.h which is under BSD-1-Clause (unbundled)
# lib/kernel/vecmath which is under GPL-3.0-or-later OR LGPL-3.0-or-later
LICENSE="MIT, BSD-1-Clause, GPL-3.0-or-later OR LGPL-3.0-or-later"
SUMMARY="OpenCL backend implementation"
DESCRIPTION="Portable Computing Language (pocl) aims to become a MIT-licensed
open source implementation of the OpenCL standard which can be easily adapted
for new targets and devices, both for homogeneous CPU and heterogenous GPUs/
accelerators. pocl uses Clang as an OpenCL C frontend and LLVM for the kernel
compiler implementation, and as a portability layer."
HOMEPAGE="http://portablecl.org/"
SRC_URI="https://github.com/pocl/pocl/archive/v${VERSION}/pocl-v${VERSION}.tar.gz"
PKG_NAMES="libpocl2 libpocl-common libpocl-devel"
libpocl2_REQUIRES="clang libpocl-common"
libpocl2_CONTENTS="
usr/bin/cygpocl-2.dll
usr/bin/libpocl-devices-basic.so
usr/bin/libpocl-devices-cuda.so
usr/bin/libpocl-devices-pthread.so
"
libpocl_common_CONTENTS="
etc/OpenCL/vendors/pocl.icd
usr/share/doc/pocl/
usr/share/pocl/
"
libpocl_devel_OBSOLETES="libpoclu-devel"
libpocl_devel_REQUIRES="libpocl-common"
libpocl_devel_CONTENTS="
usr/bin/poclcc.exe
usr/lib/libpocl.dll.a
usr/lib/pkgconfig/pocl.pc
usr/lib/pocl/cygllvmopencl.dll
usr/lib/libpocl-devices-basic.dll.a
usr/lib/libpocl-devices-cuda.dll.a
usr/lib/libpocl-devices-pthread.dll.a
"
DIFF_EXCLUDES="cl.hpp* testsuite"
CYGCMAKE_ARGS="
-DPOCL_INSTALL_ICD_VENDORDIR=/etc/OpenCL/vendors
-DPOCL_ICD_ABSOLUTE_PATH=OFF
-DENABLE_ICD=ON
-DENABLE_LIBLLVMOPENCL=ON
-DENABLE_CUDA=ON
-DCMAKE_INSTALL_PREFIX=/usr
"
[-- Attachment #3: pocl-3.1-1.src.patch --]
[-- Type: text/plain, Size: 9892 bytes --]
--- origsrc/pocl-3.1/CMakeLists.txt 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/CMakeLists.txt 2024-01-02 08:55:53.483796100 +0900
@@ -817,9 +819,9 @@ endif()
# constant addrspace variables, and stack protector likely slows
# down the kernels, so it needs to be determined whether it's worth
# the trouble.
-set(DEFAULT_KERNEL_CL_FLAGS "-xcl -fno-stack-protector -fPIC ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
-set(DEFAULT_KERNEL_C_FLAGS "-xc -std=c11 -D__CBUILD__ -fno-math-errno -fno-stack-protector -fPIC ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
-set(DEFAULT_KERNEL_CXX_FLAGS "-xc++ -std=c++11 -fno-stack-protector -fPIC ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
+set(DEFAULT_KERNEL_CL_FLAGS "-xcl -fno-stack-protector ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
+set(DEFAULT_KERNEL_C_FLAGS "-xc -std=c11 -D__CBUILD__ -fno-math-errno -fno-stack-protector ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
+set(DEFAULT_KERNEL_CXX_FLAGS "-xc++ -std=c++11 -fno-stack-protector ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
set(EXTRA_KERNEL_FLAGS "" CACHE STRING "Extra arguments to all kernel compilation commands (defaults to empty)")
@@ -883,11 +885,12 @@ if(ENABLE_SPIR)
endif()
# required for the wrapper generator
- if(CMAKE_VERSION VERSION_LESS 3.12.0)
- find_program(Python3_EXECUTABLE NAMES "python3" REQUIRED)
- else()
- find_package(Python3 REQUIRED COMPONENTS Interpreter)
- endif()
+ #if(CMAKE_VERSION VERSION_LESS 3.12.0)
+ # find_program(Python3_EXECUTABLE NAMES "python3" REQUIRED)
+ #else()
+ # find_package(Python3 REQUIRED COMPONENTS Interpreter)
+ #endif()
+ set(Python3_EXECUTABLE "/usr/bin/python3")
endif()
--- origsrc/pocl-3.1/cmake/LLVM.cmake 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/cmake/LLVM.cmake 2024-01-02 08:17:57.230897700 +0900
@@ -287,7 +287,7 @@ endforeach()
macro(find_program_or_die OUTPUT_VAR PROG_NAME DOCSTRING)
find_program(${OUTPUT_VAR}
- NAMES "${PROG_NAME}${LLVM_BINARY_SUFFIX}${CMAKE_EXECUTABLE_SUFFIX}" "${PROG_NAME}${CMAKE_EXECUTABLE_SUFFIX}"
+ NAMES "${PROG_NAME}${LLVM_BINARY_SUFFIX}" "${PROG_NAME}"
HINTS "${LLVM_BINDIR}" "${LLVM_CONFIG_LOCATION}" "${LLVM_PREFIX}" "${LLVM_PREFIX_BIN}"
DOC "${DOCSTRING}"
NO_CMAKE_PATH
--- origsrc/pocl-3.1/lib/CL/CMakeLists.txt 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/CMakeLists.txt 2024-01-02 08:17:57.233896100 +0900
@@ -294,9 +294,10 @@ set_target_properties("${POCL_LIBRARY_NA
target_link_libraries("${POCL_LIBRARY_NAME}" PRIVATE ${POCL_PRIVATE_LINK_LIST})
install(TARGETS "${POCL_LIBRARY_NAME}"
- ARCHIVE DESTINATION ${POCL_INSTALL_PUBLIC_LIBDIR}/static
+ ARCHIVE DESTINATION ${POCL_INSTALL_PUBLIC_LIBDIR}
COMPONENT "dev"
LIBRARY DESTINATION ${POCL_INSTALL_PUBLIC_LIBDIR}
+ RUNTIME DESTINATION ${POCL_INSTALL_PUBLIC_BINDIR}
COMPONENT "lib"
)
--- origsrc/pocl-3.1/lib/CL/devices/cuda/CMakeLists.txt 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/cuda/CMakeLists.txt 2024-01-02 08:54:26.135685300 +0900
@@ -23,8 +23,11 @@
#
#=============================================================================
-find_package(CUDA REQUIRED)
+find_program(CUDA_EXECUTABLE nvcc REQUIRED)
+get_filename_component(CUDA_TOOLKIT_BIN_DIR "${CUDA_EXECUTABLE}" DIRECTORY)
+set(CUDA_TOOLKIT_ROOT_DIR "${CUDA_TOOLKIT_BIN_DIR}/..")
message(STATUS "CUDA_TOOLKIT_ROOT_DIR = ${CUDA_TOOLKIT_ROOT_DIR}")
+set(CUDA_INCLUDE_DIRS "${CUDA_TOOLKIT_ROOT_DIR}/include")
set(CMAKE_CXX_FLAGS "${CMAKE_CXX_FLAGS} ${LLVM_CXXFLAGS}")
include_directories(${LLVM_INCLUDE_DIRS} ${CUDA_INCLUDE_DIRS} ${CMAKE_CURRENT_SOURCE_DIR}/../../../llvmopencl)
@@ -32,7 +36,12 @@ include_directories(${LLVM_INCLUDE_DIRS}
add_pocl_device_library("pocl-devices-cuda" pocl-cuda.c pocl-cuda.h pocl-ptx-gen.cc pocl-ptx-gen.h)
target_compile_definitions("pocl-devices-cuda" PRIVATE "-DCUDA_TOOLKIT_ROOT_DIR=\"${CUDA_TOOLKIT_ROOT_DIR}\"")
if(ENABLE_LOADABLE_DRIVERS)
- target_link_libraries(pocl-devices-cuda PRIVATE cuda ${POCL_LLVM_LIBS} ${PTHREAD_LIBRARY})
+ if (X86_64)
+ set(CUDA_LIB_ARCH "x64")
+ else()
+ set(CUDA_LIB_ARCH "Win32")
+ endif()
+ target_link_libraries(pocl-devices-cuda PRIVATE ${CUDA_TOOLKIT_ROOT_DIR}/lib/${CUDA_LIB_ARCH}/cuda.lib ${POCL_LLVM_LIBS} ${PTHREAD_LIBRARY})
endif()
if(ENABLE_CUDNN)
--- origsrc/pocl-3.1/lib/CL/devices/cuda/pocl-cuda.c 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/cuda/pocl-cuda.c 2024-01-02 08:17:57.239883300 +0900
@@ -73,6 +73,10 @@ cudnnHandle_t cudnn;
} \
}
+#ifdef __CYGWIN__
+#undef POCL_DEBUG_MESSAGES
+#endif
+
typedef struct pocl_cuda_device_data_s
{
CUdevice device;
@@ -567,6 +571,9 @@ pocl_cuda_init_queue (cl_device_id devic
queue_data->use_threads
= !pocl_get_bool_option ("POCL_CUDA_DISABLE_QUEUE_THREADS", 1);
+#ifdef __CYGWIN__
+ queue_data->use_threads = 0; /* Thread does not work in windows CUDA */
+#endif
if (queue_data->use_threads)
{
@@ -2107,7 +2114,8 @@ pocl_cuda_free_event_data (cl_event even
{
pocl_cuda_event_data_t *event_data
= (pocl_cuda_event_data_t *)event->data;
- PTHREAD_CHECK (pthread_cond_destroy (&event_data->event_cond));
+ if (event_data->event_cond)
+ PTHREAD_CHECK (pthread_cond_destroy (&event_data->event_cond));
if (event->queue->properties & CL_QUEUE_PROFILING_ENABLE)
cuEventDestroy (event_data->start);
cuEventDestroy (event_data->end);
--- origsrc/pocl-3.1/lib/CL/devices/cuda/pocl-ptx-gen.cc 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/cuda/pocl-ptx-gen.cc 2024-01-02 08:17:57.241882300 +0900
@@ -960,11 +960,19 @@ int pocl_cuda_get_ptr_arg_alignment(cons
llvm::dyn_cast<llvm::GetElementPtrInst>(U)) {
for (auto UU : GEP->users()) {
if (llvm::StoreInst *SI = llvm::dyn_cast<llvm::StoreInst>(UU)) {
+#ifdef LLVM_OLDER_THAN_15_0
+ Alignments[i] = SI->getAlignment();
+#else
Alignments[i] = SI->getAlign().value();
+#endif
break;
}
if (llvm::LoadInst *LI = llvm::dyn_cast<llvm::LoadInst>(UU)) {
+#ifdef LLVM_OLDER_THAN_15_0
+ Alignments[i] = LI->getAlignment();
+#else
Alignments[i] = LI->getAlign().value();
+#endif
break;
}
}
--- origsrc/pocl-3.1/lib/CL/devices/topology/pocl_topology.c 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/topology/pocl_topology.c 2024-01-02 08:17:57.244880900 +0900
@@ -205,7 +205,7 @@ exit_destroy:
}
// #ifdef HWLOC
-#elif defined(__linux__) || defined(__ANDROID__)
+#elif defined(__linux__) || defined(__ANDROID__) || defined(__CYGWIN__)
#define L3_CACHE_SIZE "/sys/devices/system/cpu/cpu0/cache/index3/size"
#define L2_CACHE_SIZE "/sys/devices/system/cpu/cpu0/cache/index2/size"
--- origsrc/pocl-3.1/lib/CL/pocl_build.c 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/pocl_build.c 2024-01-02 10:47:45.937257900 +0900
@@ -690,6 +690,13 @@ compile_and_link_program(int compile_pro
goto ERROR_CLEAN_OPTIONS;
}
+#ifdef __CYGWIN__
+ if (program->compiler_options == NULL)
+ {
+ program->compiler_options = (char *)malloc(512);
+ program->compiler_options[0] = '\0';
+ }
+#endif
POCL_MSG_PRINT_LLVM ("building program with options %s\n",
program->compiler_options);
--- origsrc/pocl-3.1/lib/CL/pocl_util.c 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/pocl_util.c 2024-01-02 08:17:57.247891900 +0900
@@ -59,8 +59,10 @@
#if defined(__APPLE__)
#define _DARWIN_C_SOURCE
#endif
-#ifdef __linux__
+#if defined(__linux__) || defined(__CYGWIN__)
#define _GNU_SOURCE
+#undef __GNU_VISIBLE
+#define __GNU_VISIBLE 1
#endif
#include <dlfcn.h>
#endif
--- origsrc/pocl-3.1/lib/kernel/host/spir_wrapper32.ll 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/kernel/host/spir_wrapper32.ll 2024-01-02 08:17:57.250886400 +0900
@@ -2663,7 +2663,7 @@ attributes #0 = { nounwind "correctly-ro
!0 = !{i32 1, i32 2}
!1 = !{!"clang version 6.0.0"}
-!2 = !{i32 1, !"wchar_size", i32 4}
+!2 = !{i32 1, !"wchar_size", i32 2}
!3 = !{i32 7, !"PIC Level", i32 2}
--- origsrc/pocl-3.1/lib/kernel/host/spir_wrapper64.ll 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/kernel/host/spir_wrapper64.ll 2024-01-02 08:17:57.255884700 +0900
@@ -14731,7 +14731,7 @@ attributes #0 = { nounwind "correctly-ro
!0 = !{i32 1, i32 2}
!1 = !{!"clang version 6.0.0"}
-!2 = !{i32 1, !"wchar_size", i32 4}
+!2 = !{i32 1, !"wchar_size", i32 2}
!3 = !{i32 7, !"PIC Level", i32 2}
--- origsrc/pocl-3.1/lib/llvmopencl/CMakeLists.txt 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/llvmopencl/CMakeLists.txt 2024-01-02 08:17:57.257883900 +0900
@@ -115,9 +115,10 @@ harden("llvmopencl")
# not sure where other platforms get their library linkage list, probably there is
# way to make this more consistent on different platforms
-if(MSVC)
+if(WIN32 OR CYGWIN)
+ target_link_libraries("llvmopencl" pocl)
target_link_libraries("llvmopencl" ${POCL_LLVM_LIBS})
-endif(MSVC)
+endif(WIN32 OR CYGWIN)
#target_link_libraries("llvmopencl" "${LLVM_SYSLIBS}")
endif(ENABLE_LIBLLVMOPENCL)
--- origsrc/pocl-3.1/lib/llvmopencl/DebugHelpers.h 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/llvmopencl/DebugHelpers.h 2024-01-02 08:17:57.260886300 +0900
@@ -24,7 +24,7 @@
#define _POCL_DEBUG_HELPERS_H
#include <string>
-#if _MSC_VER
+#if _MSC_VER || defined(__CYGWIN__)
# include <set>
#endif
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 5:14 [ITA] pocl Takashi Yano
@ 2024-01-03 5:25 ` Takashi Yano
2024-01-03 7:54 ` Marco Atzeri
0 siblings, 1 reply; 18+ messages in thread
From: Takashi Yano @ 2024-01-03 5:25 UTC (permalink / raw)
To: cygwin-apps
On Wed, 3 Jan 2024 14:14:12 +0900
Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
> I'd like to adopt the pocl package.
>
> - Update to latest upstream release.
Sorry, the latest upstream release is 5.0 however, 4.0 and later
cannot be built in current cygwin because LLVM package is old.
This update is up to 3.1.
> - Enable CUDA support.
--
Takashi Yano <takashi.yano@nifty.ne.jp>
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 5:25 ` Takashi Yano
@ 2024-01-03 7:54 ` Marco Atzeri
2024-01-03 9:29 ` Takashi Yano
2024-01-08 0:38 ` Andrew Schulman
0 siblings, 2 replies; 18+ messages in thread
From: Marco Atzeri @ 2024-01-03 7:54 UTC (permalink / raw)
To: cygwin-apps
On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
> On Wed, 3 Jan 2024 14:14:12 +0900
> Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
>> I'd like to adopt the pocl package.
>>
>> - Update to latest upstream release.
$ git diff |grep "^+"
+++ b/cygwin-pkg-maint
+pocl Takashi Yano
> Sorry, the latest upstream release is 5.0 however, 4.0 and later
> cannot be built in current cygwin because LLVM package is old.
> This update is up to 3.1.
>
>> - Enable CUDA support.
Curiosity, how do we support CUDA on Cygwin ?
Regards
Marco
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 7:54 ` Marco Atzeri
@ 2024-01-03 9:29 ` Takashi Yano
2024-01-03 11:38 ` Brian Inglis
2024-01-07 12:51 ` Jon Turney
2024-01-08 0:38 ` Andrew Schulman
1 sibling, 2 replies; 18+ messages in thread
From: Takashi Yano @ 2024-01-03 9:29 UTC (permalink / raw)
To: cygwin-apps
On Wed, 3 Jan 2024 08:54:17 +0100
Marco Atzeri wrote:
> On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
> > On Wed, 3 Jan 2024 14:14:12 +0900
> > Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
> >> I'd like to adopt the pocl package.
> >>
> >> - Update to latest upstream release.
>
> $ git diff |grep "^+"
> +++ b/cygwin-pkg-maint
> +pocl Takashi Yano
Thanks!
> > Sorry, the latest upstream release is 5.0 however, 4.0 and later
> > cannot be built in current cygwin because LLVM package is old.
> > This update is up to 3.1.
> >
> >> - Enable CUDA support.
>
> Curiosity, how do we support CUDA on Cygwin ?
nvidia cuda toolkit is used in build stage of user programs.
Although this is not very desirable for cygwin package, I thought
that the advantage of being able to use the GPU was greater than
the disadvantage.
However, on the second thought, cuda support should be a separeted
package from the base package, and suggest installing cuda toolkit
in the install stage of of that package.
Let me consider a bit. If you have any idea, please let me know.
--
Takashi Yano <takashi.yano@nifty.ne.jp>
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 9:29 ` Takashi Yano
@ 2024-01-03 11:38 ` Brian Inglis
2024-01-03 12:00 ` Takashi Yano
2024-01-07 12:51 ` Jon Turney
1 sibling, 1 reply; 18+ messages in thread
From: Brian Inglis @ 2024-01-03 11:38 UTC (permalink / raw)
To: cygwin-apps
On 2024-01-03 02:29, Takashi Yano via Cygwin-apps wrote:
> On Wed, 3 Jan 2024 08:54:17 +0100
> Marco Atzeri wrote:
>> On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
>>> On Wed, 3 Jan 2024 14:14:12 +0900
>>> Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
>>>> I'd like to adopt the pocl package.
>>>> - Update to latest upstream release.
>> $ git diff |grep "^+"
>> +++ b/cygwin-pkg-maint
>> +pocl Takashi Yano
>>> Sorry, the latest upstream release is 5.0 however, 4.0 and later
>>> cannot be built in current cygwin because LLVM package is old.
>>> This update is up to 3.1.
>>>> - Enable CUDA support.
>> Curiosity, how do we support CUDA on Cygwin ?
> nvidia cuda toolkit is used in build stage of user programs.
> Although this is not very desirable for cygwin package, I thought
> that the advantage of being able to use the GPU was greater than
> the disadvantage.
> However, on the second thought, cuda support should be a separeted
> package from the base package, and suggest installing cuda toolkit
> in the install stage of of that package.
> Let me consider a bit. If you have any idea, please let me know.
Please note CUDA is Nvidia proprietary closed source - I do not think we can or
should touch it when OpenCL 3+ supports Nvidia devices.
Fedora does not support CUDA although others do in their non-free "sources".
--
Take care. Thanks, Brian Inglis Calgary, Alberta, Canada
La perfection est atteinte Perfection is achieved
non pas lorsqu'il n'y a plus rien à ajouter not when there is no more to add
mais lorsqu'il n'y a plus rien à retirer but when there is no more to cut
-- Antoine de Saint-Exupéry
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 11:38 ` Brian Inglis
@ 2024-01-03 12:00 ` Takashi Yano
2024-01-03 12:26 ` Brian Inglis
2024-01-03 12:30 ` Takashi Yano
0 siblings, 2 replies; 18+ messages in thread
From: Takashi Yano @ 2024-01-03 12:00 UTC (permalink / raw)
To: cygwin-apps
On Wed, 3 Jan 2024 04:38:02 -0700
Brian Inglis wrote:
> On 2024-01-03 02:29, Takashi Yano via Cygwin-apps wrote:
> > On Wed, 3 Jan 2024 08:54:17 +0100
> > Marco Atzeri wrote:
> >> On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
> >>> On Wed, 3 Jan 2024 14:14:12 +0900
> >>> Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
> >>>> I'd like to adopt the pocl package.
> >>>> - Update to latest upstream release.
>
> >> $ git diff |grep "^+"
> >> +++ b/cygwin-pkg-maint
> >> +pocl Takashi Yano
>
> >>> Sorry, the latest upstream release is 5.0 however, 4.0 and later
> >>> cannot be built in current cygwin because LLVM package is old.
> >>> This update is up to 3.1.
>
> >>>> - Enable CUDA support.
>
> >> Curiosity, how do we support CUDA on Cygwin ?
>
> > nvidia cuda toolkit is used in build stage of user programs.
> > Although this is not very desirable for cygwin package, I thought
> > that the advantage of being able to use the GPU was greater than
> > the disadvantage.
> > However, on the second thought, cuda support should be a separeted
> > package from the base package, and suggest installing cuda toolkit
> > in the install stage of of that package.
> > Let me consider a bit. If you have any idea, please let me know.
>
> Please note CUDA is Nvidia proprietary closed source - I do not think we can or
> should touch it when OpenCL 3+ supports Nvidia devices.
> Fedora does not support CUDA although others do in their non-free "sources".
We do not touch CUDA itself or distribute its binaries, but just use binaries
distributed by NVIDIA. Source code in pocl is not NVIDIA proprietary. In that
sense, cygwin itself uses microsoft proprietary closed source modules.
So, enabling CUDA support in pocl should also be allowed, I think.
--
Takashi Yano <takashi.yano@nifty.ne.jp>
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 12:00 ` Takashi Yano
@ 2024-01-03 12:26 ` Brian Inglis
2024-01-03 12:42 ` Takashi Yano
2024-01-03 12:30 ` Takashi Yano
1 sibling, 1 reply; 18+ messages in thread
From: Brian Inglis @ 2024-01-03 12:26 UTC (permalink / raw)
To: cygwin-apps
On 2024-01-03 05:00, Takashi Yano via Cygwin-apps wrote:
> On Wed, 3 Jan 2024 04:38:02 -0700
> Brian Inglis wrote:
>> On 2024-01-03 02:29, Takashi Yano via Cygwin-apps wrote:
>>> On Wed, 3 Jan 2024 08:54:17 +0100
>>> Marco Atzeri wrote:
>>>> On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
>>>>> On Wed, 3 Jan 2024 14:14:12 +0900
>>>>> Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
>>>>>> I'd like to adopt the pocl package.
>>>>>> - Update to latest upstream release.
>>
>>>> $ git diff |grep "^+"
>>>> +++ b/cygwin-pkg-maint
>>>> +pocl Takashi Yano
>>
>>>>> Sorry, the latest upstream release is 5.0 however, 4.0 and later
>>>>> cannot be built in current cygwin because LLVM package is old.
>>>>> This update is up to 3.1.
>>
>>>>>> - Enable CUDA support.
>>
>>>> Curiosity, how do we support CUDA on Cygwin ?
>>
>>> nvidia cuda toolkit is used in build stage of user programs.
>>> Although this is not very desirable for cygwin package, I thought
>>> that the advantage of being able to use the GPU was greater than
>>> the disadvantage.
>>> However, on the second thought, cuda support should be a separeted
>>> package from the base package, and suggest installing cuda toolkit
>>> in the install stage of of that package.
>>> Let me consider a bit. If you have any idea, please let me know.
>>
>> Please note CUDA is Nvidia proprietary closed source - I do not think we can or
>> should touch it when OpenCL 3+ supports Nvidia devices.
>> Fedora does not support CUDA although others do in their non-free "sources".
>
> We do not touch CUDA itself or distribute its binaries, but just use binaries
> distributed by NVIDIA. Source code in pocl is not NVIDIA proprietary. In that
> sense, cygwin itself uses microsoft proprietary closed source modules.
Cygwin provides and runs open source tools, headers, and libraries to perform
the builds and execution, calling proprietary interfaces to support POSIX.
> So, enabling CUDA support in pocl should also be allowed, I think.
I believe not if the Nvidia tools do not have sources available to build with
Cygwin tools built from sources.
--
Take care. Thanks, Brian Inglis Calgary, Alberta, Canada
La perfection est atteinte Perfection is achieved
non pas lorsqu'il n'y a plus rien à ajouter not when there is no more to add
mais lorsqu'il n'y a plus rien à retirer but when there is no more to cut
-- Antoine de Saint-Exupéry
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 12:00 ` Takashi Yano
2024-01-03 12:26 ` Brian Inglis
@ 2024-01-03 12:30 ` Takashi Yano
2024-01-03 14:08 ` Takashi Yano
1 sibling, 1 reply; 18+ messages in thread
From: Takashi Yano @ 2024-01-03 12:30 UTC (permalink / raw)
To: cygwin-apps
On Wed, 3 Jan 2024 21:00:07 +0900
Takashi Yano wrote:
> On Wed, 3 Jan 2024 04:38:02 -0700
> Brian Inglis wrote:
> > On 2024-01-03 02:29, Takashi Yano via Cygwin-apps wrote:
> > > On Wed, 3 Jan 2024 08:54:17 +0100
> > > Marco Atzeri wrote:
> > >> On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
> > >>> On Wed, 3 Jan 2024 14:14:12 +0900
> > >>> Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
> > >>>> I'd like to adopt the pocl package.
> > >>>> - Update to latest upstream release.
> >
> > >> $ git diff |grep "^+"
> > >> +++ b/cygwin-pkg-maint
> > >> +pocl Takashi Yano
> >
> > >>> Sorry, the latest upstream release is 5.0 however, 4.0 and later
> > >>> cannot be built in current cygwin because LLVM package is old.
> > >>> This update is up to 3.1.
> >
> > >>>> - Enable CUDA support.
> >
> > >> Curiosity, how do we support CUDA on Cygwin ?
> >
> > > nvidia cuda toolkit is used in build stage of user programs.
> > > Although this is not very desirable for cygwin package, I thought
> > > that the advantage of being able to use the GPU was greater than
> > > the disadvantage.
> > > However, on the second thought, cuda support should be a separeted
> > > package from the base package, and suggest installing cuda toolkit
> > > in the install stage of of that package.
> > > Let me consider a bit. If you have any idea, please let me know.
> >
> > Please note CUDA is Nvidia proprietary closed source - I do not think we can or
> > should touch it when OpenCL 3+ supports Nvidia devices.
> > Fedora does not support CUDA although others do in their non-free "sources".
>
> We do not touch CUDA itself or distribute its binaries, but just use binaries
> distributed by NVIDIA. Source code in pocl is not NVIDIA proprietary. In that
> sense, cygwin itself uses microsoft proprietary closed source modules.
>
> So, enabling CUDA support in pocl should also be allowed, I think.
D'oh! I missed that libpocl-devices-cuda.so is linked with cuda.lib
from CUDA Toolkit.
I'll give up enabling CUDA support for pocl.
Thanks!
--
Takashi Yano <takashi.yano@nifty.ne.jp>
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 12:26 ` Brian Inglis
@ 2024-01-03 12:42 ` Takashi Yano
0 siblings, 0 replies; 18+ messages in thread
From: Takashi Yano @ 2024-01-03 12:42 UTC (permalink / raw)
To: cygwin-apps
On Wed, 3 Jan 2024 05:26:43 -0700
Brian Inglis wrote:
> On 2024-01-03 05:00, Takashi Yano via Cygwin-apps wrote:
> > On Wed, 3 Jan 2024 04:38:02 -0700
> > Brian Inglis wrote:
> >> On 2024-01-03 02:29, Takashi Yano via Cygwin-apps wrote:
> >>> On Wed, 3 Jan 2024 08:54:17 +0100
> >>> Marco Atzeri wrote:
> >>>> On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
> >>>>> On Wed, 3 Jan 2024 14:14:12 +0900
> >>>>> Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
> >>>>>> I'd like to adopt the pocl package.
> >>>>>> - Update to latest upstream release.
> >>
> >>>> $ git diff |grep "^+"
> >>>> +++ b/cygwin-pkg-maint
> >>>> +pocl Takashi Yano
> >>
> >>>>> Sorry, the latest upstream release is 5.0 however, 4.0 and later
> >>>>> cannot be built in current cygwin because LLVM package is old.
> >>>>> This update is up to 3.1.
> >>
> >>>>>> - Enable CUDA support.
> >>
> >>>> Curiosity, how do we support CUDA on Cygwin ?
> >>
> >>> nvidia cuda toolkit is used in build stage of user programs.
> >>> Although this is not very desirable for cygwin package, I thought
> >>> that the advantage of being able to use the GPU was greater than
> >>> the disadvantage.
> >>> However, on the second thought, cuda support should be a separeted
> >>> package from the base package, and suggest installing cuda toolkit
> >>> in the install stage of of that package.
> >>> Let me consider a bit. If you have any idea, please let me know.
> >>
> >> Please note CUDA is Nvidia proprietary closed source - I do not think we can or
> >> should touch it when OpenCL 3+ supports Nvidia devices.
> >> Fedora does not support CUDA although others do in their non-free "sources".
> >
> > We do not touch CUDA itself or distribute its binaries, but just use binaries
> > distributed by NVIDIA. Source code in pocl is not NVIDIA proprietary. In that
> > sense, cygwin itself uses microsoft proprietary closed source modules.
>
> Cygwin provides and runs open source tools, headers, and libraries to perform
> the builds and execution, calling proprietary interfaces to support POSIX.
I meant cygwin1.dll calls kernel32.dll which is not open source
just like pocl with CUDA support calls nvcc.exe.
--
Takashi Yano <takashi.yano@nifty.ne.jp>
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 12:30 ` Takashi Yano
@ 2024-01-03 14:08 ` Takashi Yano
2024-01-04 0:55 ` Takashi Yano
0 siblings, 1 reply; 18+ messages in thread
From: Takashi Yano @ 2024-01-03 14:08 UTC (permalink / raw)
To: cygwin-apps
On Wed, 3 Jan 2024 21:30:02 +0900
Takashi Yano wrote:
> On Wed, 3 Jan 2024 21:00:07 +0900
> Takashi Yano wrote:
> > On Wed, 3 Jan 2024 04:38:02 -0700
> > Brian Inglis wrote:
> > > On 2024-01-03 02:29, Takashi Yano via Cygwin-apps wrote:
> > > > On Wed, 3 Jan 2024 08:54:17 +0100
> > > > Marco Atzeri wrote:
> > > >> On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
> > > >>> On Wed, 3 Jan 2024 14:14:12 +0900
> > > >>> Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
> > > >>>> I'd like to adopt the pocl package.
> > > >>>> - Update to latest upstream release.
> > >
> > > >> $ git diff |grep "^+"
> > > >> +++ b/cygwin-pkg-maint
> > > >> +pocl Takashi Yano
> > >
> > > >>> Sorry, the latest upstream release is 5.0 however, 4.0 and later
> > > >>> cannot be built in current cygwin because LLVM package is old.
> > > >>> This update is up to 3.1.
> > >
> > > >>>> - Enable CUDA support.
> > >
> > > >> Curiosity, how do we support CUDA on Cygwin ?
> > >
> > > > nvidia cuda toolkit is used in build stage of user programs.
> > > > Although this is not very desirable for cygwin package, I thought
> > > > that the advantage of being able to use the GPU was greater than
> > > > the disadvantage.
> > > > However, on the second thought, cuda support should be a separeted
> > > > package from the base package, and suggest installing cuda toolkit
> > > > in the install stage of of that package.
> > > > Let me consider a bit. If you have any idea, please let me know.
> > >
> > > Please note CUDA is Nvidia proprietary closed source - I do not think we can or
> > > should touch it when OpenCL 3+ supports Nvidia devices.
> > > Fedora does not support CUDA although others do in their non-free "sources".
> >
> > We do not touch CUDA itself or distribute its binaries, but just use binaries
> > distributed by NVIDIA. Source code in pocl is not NVIDIA proprietary. In that
> > sense, cygwin itself uses microsoft proprietary closed source modules.
> >
> > So, enabling CUDA support in pocl should also be allowed, I think.
>
> D'oh! I missed that libpocl-devices-cuda.so is linked with cuda.lib
> from CUDA Toolkit.
>
> I'll give up enabling CUDA support for pocl.
Ah, cuda.lib is just a import library for nvcuda.dll, so
we can easily create non-proprietary import library using
dlltool.
Then, libpocl-devices-cuda.so will be free from NVIDIA binaries
just like libkernel32.a of w32api-runtime.
--
Takashi Yano <takashi.yano@nifty.ne.jp>
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 14:08 ` Takashi Yano
@ 2024-01-04 0:55 ` Takashi Yano
2024-01-13 15:48 ` Jon Turney
0 siblings, 1 reply; 18+ messages in thread
From: Takashi Yano @ 2024-01-04 0:55 UTC (permalink / raw)
To: cygwin-apps
[-- Attachment #1: Type: text/plain, Size: 3431 bytes --]
On Wed, 3 Jan 2024 23:08:27 +0900
Takashi Yano wrote:
> On Wed, 3 Jan 2024 21:30:02 +0900
> Takashi Yano wrote:
> > On Wed, 3 Jan 2024 21:00:07 +0900
> > Takashi Yano wrote:
> > > On Wed, 3 Jan 2024 04:38:02 -0700
> > > Brian Inglis wrote:
> > > > On 2024-01-03 02:29, Takashi Yano via Cygwin-apps wrote:
> > > > > On Wed, 3 Jan 2024 08:54:17 +0100
> > > > > Marco Atzeri wrote:
> > > > >> On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
> > > > >>> On Wed, 3 Jan 2024 14:14:12 +0900
> > > > >>> Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
> > > > >>>> I'd like to adopt the pocl package.
> > > > >>>> - Update to latest upstream release.
> > > >
> > > > >> $ git diff |grep "^+"
> > > > >> +++ b/cygwin-pkg-maint
> > > > >> +pocl Takashi Yano
> > > >
> > > > >>> Sorry, the latest upstream release is 5.0 however, 4.0 and later
> > > > >>> cannot be built in current cygwin because LLVM package is old.
> > > > >>> This update is up to 3.1.
> > > >
> > > > >>>> - Enable CUDA support.
> > > >
> > > > >> Curiosity, how do we support CUDA on Cygwin ?
> > > >
> > > > > nvidia cuda toolkit is used in build stage of user programs.
> > > > > Although this is not very desirable for cygwin package, I thought
> > > > > that the advantage of being able to use the GPU was greater than
> > > > > the disadvantage.
> > > > > However, on the second thought, cuda support should be a separeted
> > > > > package from the base package, and suggest installing cuda toolkit
> > > > > in the install stage of of that package.
> > > > > Let me consider a bit. If you have any idea, please let me know.
> > > >
> > > > Please note CUDA is Nvidia proprietary closed source - I do not think we can or
> > > > should touch it when OpenCL 3+ supports Nvidia devices.
> > > > Fedora does not support CUDA although others do in their non-free "sources".
> > >
> > > We do not touch CUDA itself or distribute its binaries, but just use binaries
> > > distributed by NVIDIA. Source code in pocl is not NVIDIA proprietary. In that
> > > sense, cygwin itself uses microsoft proprietary closed source modules.
> > >
> > > So, enabling CUDA support in pocl should also be allowed, I think.
> >
> > D'oh! I missed that libpocl-devices-cuda.so is linked with cuda.lib
> > from CUDA Toolkit.
> >
> > I'll give up enabling CUDA support for pocl.
>
> Ah, cuda.lib is just a import library for nvcuda.dll, so
> we can easily create non-proprietary import library using
> dlltool.
>
> Then, libpocl-devices-cuda.so will be free from NVIDIA binaries
> just like libkernel32.a of w32api-runtime.
Package files are revised.
- Stop to link libpocl-devices-cuda.so against cuda.lib which is
a part of CUDA Toolkit. Instead, self-built import library (i.e.
libcuda.a) for nvcuda.dll is used just like libkernel32.a in
cygwin1.dll.
Now, the package itself is completely free from CUDA Toolkit. Only
user programs which use CUDA need the toolkit at the first execution
time to build the kernel objects. If no CUDA Toolkit is found at
this time, the message:
"[CUDA] failed to open libdevice library file. Most likely, you do
not have NVIDIA CUDA Toolkit. Please consider to install it. If you
have it installed, set CUDA_PATH properly."
will be shown.
Any comments and advices will be appreciated.
--
Takashi Yano <takashi.yano@nifty.ne.jp>
[-- Attachment #2: pocl.cygport --]
[-- Type: text/plain, Size: 1770 bytes --]
inherit clang cmake
NAME="pocl"
VERSION=3.1
RELEASE=1
CATEGORY="Libs"
# The entire code is under MIT
# include/utlist.h which is under BSD-1-Clause (unbundled)
# lib/kernel/vecmath which is under GPL-3.0-or-later OR LGPL-3.0-or-later
LICENSE="MIT, BSD-1-Clause, GPL-3.0-or-later OR LGPL-3.0-or-later"
SUMMARY="OpenCL backend implementation"
DESCRIPTION="Portable Computing Language (pocl) aims to become a MIT-licensed
open source implementation of the OpenCL standard which can be easily adapted
for new targets and devices, both for homogeneous CPU and heterogenous GPUs/
accelerators. pocl uses Clang as an OpenCL C frontend and LLVM for the kernel
compiler implementation, and as a portability layer."
HOMEPAGE="http://portablecl.org/"
SRC_URI="https://github.com/pocl/pocl/archive/v${VERSION}/pocl-v${VERSION}.tar.gz"
PKG_NAMES="libpocl2 libpocl-common libpocl-devel"
libpocl2_REQUIRES="clang libpocl-common"
libpocl2_CONTENTS="
usr/bin/cygpocl-2.dll
usr/bin/libpocl-devices-basic.so
usr/bin/libpocl-devices-cuda.so
usr/bin/libpocl-devices-pthread.so
"
libpocl_common_CONTENTS="
etc/OpenCL/vendors/pocl.icd
usr/share/doc/pocl/
usr/share/pocl/
"
libpocl_devel_OBSOLETES="libpoclu-devel"
libpocl_devel_REQUIRES="libpocl-common libpocl2"
libpocl_devel_CONTENTS="
usr/bin/poclcc.exe
usr/lib/libpocl.dll.a
usr/lib/pkgconfig/pocl.pc
usr/lib/pocl/cygllvmopencl.dll
usr/lib/libpocl-devices-basic.dll.a
usr/lib/libpocl-devices-cuda.dll.a
usr/lib/libpocl-devices-pthread.dll.a
"
DIFF_EXCLUDES="cl.hpp* testsuite"
CYGCMAKE_ARGS="
-DPOCL_INSTALL_ICD_VENDORDIR=/etc/OpenCL/vendors
-DPOCL_ICD_ABSOLUTE_PATH=OFF
-DENABLE_ICD=ON
-DENABLE_LIBLLVMOPENCL=ON
-DENABLE_CUDA=ON
-DCMAKE_INSTALL_PREFIX=/usr
"
[-- Attachment #3: pocl-3.1-1.src.patch --]
[-- Type: text/plain, Size: 31976 bytes --]
--- origsrc/pocl-3.1/CMakeLists.txt 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/CMakeLists.txt 2024-01-04 03:05:15.035161600 +0900
@@ -817,9 +817,9 @@ endif()
# constant addrspace variables, and stack protector likely slows
# down the kernels, so it needs to be determined whether it's worth
# the trouble.
-set(DEFAULT_KERNEL_CL_FLAGS "-xcl -fno-stack-protector -fPIC ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
-set(DEFAULT_KERNEL_C_FLAGS "-xc -std=c11 -D__CBUILD__ -fno-math-errno -fno-stack-protector -fPIC ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
-set(DEFAULT_KERNEL_CXX_FLAGS "-xc++ -std=c++11 -fno-stack-protector -fPIC ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
+set(DEFAULT_KERNEL_CL_FLAGS "-xcl -fno-stack-protector ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
+set(DEFAULT_KERNEL_C_FLAGS "-xc -std=c11 -D__CBUILD__ -fno-math-errno -fno-stack-protector ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
+set(DEFAULT_KERNEL_CXX_FLAGS "-xc++ -std=c++11 -fno-stack-protector ${FLOATCONV_FLAG} ${OPAQUE_PTR_FLAGS}")
set(EXTRA_KERNEL_FLAGS "" CACHE STRING "Extra arguments to all kernel compilation commands (defaults to empty)")
@@ -883,11 +883,12 @@ if(ENABLE_SPIR)
endif()
# required for the wrapper generator
- if(CMAKE_VERSION VERSION_LESS 3.12.0)
- find_program(Python3_EXECUTABLE NAMES "python3" REQUIRED)
- else()
- find_package(Python3 REQUIRED COMPONENTS Interpreter)
- endif()
+ #if(CMAKE_VERSION VERSION_LESS 3.12.0)
+ # find_program(Python3_EXECUTABLE NAMES "python3" REQUIRED)
+ #else()
+ # find_package(Python3 REQUIRED COMPONENTS Interpreter)
+ #endif()
+ set(Python3_EXECUTABLE "/usr/bin/python3")
endif()
--- origsrc/pocl-3.1/cmake/LLVM.cmake 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/cmake/LLVM.cmake 2024-01-04 03:05:15.037160500 +0900
@@ -287,7 +287,7 @@ endforeach()
macro(find_program_or_die OUTPUT_VAR PROG_NAME DOCSTRING)
find_program(${OUTPUT_VAR}
- NAMES "${PROG_NAME}${LLVM_BINARY_SUFFIX}${CMAKE_EXECUTABLE_SUFFIX}" "${PROG_NAME}${CMAKE_EXECUTABLE_SUFFIX}"
+ NAMES "${PROG_NAME}${LLVM_BINARY_SUFFIX}" "${PROG_NAME}"
HINTS "${LLVM_BINDIR}" "${LLVM_CONFIG_LOCATION}" "${LLVM_PREFIX}" "${LLVM_PREFIX_BIN}"
DOC "${DOCSTRING}"
NO_CMAKE_PATH
--- origsrc/pocl-3.1/lib/CL/CMakeLists.txt 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/CMakeLists.txt 2024-01-04 03:05:15.040159200 +0900
@@ -294,9 +294,10 @@ set_target_properties("${POCL_LIBRARY_NA
target_link_libraries("${POCL_LIBRARY_NAME}" PRIVATE ${POCL_PRIVATE_LINK_LIST})
install(TARGETS "${POCL_LIBRARY_NAME}"
- ARCHIVE DESTINATION ${POCL_INSTALL_PUBLIC_LIBDIR}/static
+ ARCHIVE DESTINATION ${POCL_INSTALL_PUBLIC_LIBDIR}
COMPONENT "dev"
LIBRARY DESTINATION ${POCL_INSTALL_PUBLIC_LIBDIR}
+ RUNTIME DESTINATION ${POCL_INSTALL_PUBLIC_BINDIR}
COMPONENT "lib"
)
--- origsrc/pocl-3.1/lib/CL/devices/cuda/CMakeLists.txt 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/cuda/CMakeLists.txt 2024-01-04 03:05:15.042157700 +0900
@@ -23,16 +23,13 @@
#
#=============================================================================
-find_package(CUDA REQUIRED)
-message(STATUS "CUDA_TOOLKIT_ROOT_DIR = ${CUDA_TOOLKIT_ROOT_DIR}")
-
set(CMAKE_CXX_FLAGS "${CMAKE_CXX_FLAGS} ${LLVM_CXXFLAGS}")
include_directories(${LLVM_INCLUDE_DIRS} ${CUDA_INCLUDE_DIRS} ${CMAKE_CURRENT_SOURCE_DIR}/../../../llvmopencl)
-add_pocl_device_library("pocl-devices-cuda" pocl-cuda.c pocl-cuda.h pocl-ptx-gen.cc pocl-ptx-gen.h)
-target_compile_definitions("pocl-devices-cuda" PRIVATE "-DCUDA_TOOLKIT_ROOT_DIR=\"${CUDA_TOOLKIT_ROOT_DIR}\"")
+add_pocl_device_library("pocl-devices-cuda" pocl-cuda.c pocl-cuda.h pocl-ptx-gen.cc pocl-ptx-gen.h cuda.h)
+add_custom_command(TARGET pocl-devices-cuda PRE_LINK COMMAND dlltool -d ${CMAKE_CURRENT_SOURCE_DIR}/nvcuda.def -D nvcuda.dll -l libcuda.a)
if(ENABLE_LOADABLE_DRIVERS)
- target_link_libraries(pocl-devices-cuda PRIVATE cuda ${POCL_LLVM_LIBS} ${PTHREAD_LIBRARY})
+ target_link_libraries(pocl-devices-cuda PRIVATE -L${CMAKE_CURRENT_BINARY_DIR} cuda ${POCL_LLVM_LIBS} ${PTHREAD_LIBRARY})
endif()
if(ENABLE_CUDNN)
--- origsrc/pocl-3.1/lib/CL/devices/cuda/cuda.h 1970-01-01 09:00:00.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/cuda/cuda.h 2024-01-04 03:05:15.046155400 +0900
@@ -0,0 +1,119 @@
+#ifndef _CUDA_H_
+#define _CUDA_H_
+typedef unsigned int CUdevice;
+typedef void *CUcontext;
+typedef void *CUevent;
+typedef void *CUstream;
+typedef void *CUmodule;
+typedef void *CUfunction;
+typedef unsigned int CUresult;
+typedef unsigned int CUdevice_attirbute;
+typedef unsigned long long CUdeviceptr;
+typedef unsigned int CUmemorytype;
+typedef void *CUarray;
+typedef unsigned int CUjit_option;
+typedef struct {
+ size_t srcXInBytes;
+ size_t srcY;
+ size_t srcZ;
+ size_t srcLOD;
+ CUmemorytype srcMemoryType;
+ const void *srcHost;
+ CUdeviceptr srcDevice;
+ CUarray srcArray;
+ void *reserved0;
+ size_t srcPitch;
+ size_t srcHeight;
+ size_t dstXInBytes;
+ size_t dstY;
+ size_t dstZ;
+ size_t dstLOD;
+ CUmemorytype dstMemoryType;
+ void *dstHost;
+ CUdeviceptr dstDevice;
+ CUarray dstArray;
+ void *reserved1;
+ size_t dstPitch;
+ size_t dstHeight;
+ size_t WidthInBytes;
+ size_t Height;
+ size_t Depth;
+} CUDA_MEMCPY3D;
+#define CUDA_SUCCESS 0
+#define CUDA_ERROR_HOST_MEMORY_ALREADY_REGISTERED 712
+#define CU_DEVICE_ATTRIBUTE_MAX_THREADS_PER_BLOCK 1
+#define CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_X 2
+#define CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_Y 3
+#define CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_Z 4
+#define CU_DEVICE_ATTRIBUTE_TOTAL_CONSTANT_MEMORY 9
+#define CU_DEVICE_ATTRIBUTE_WARP_SIZE 10
+#define CU_DEVICE_ATTRIBUTE_MAX_REGISTERS_PER_BLOCK 12
+#define CU_DEVICE_ATTRIBUTE_CLOCK_RATE 13
+#define CU_DEVICE_ATTRIBUTE_TEXTURE_ALIGNMENT 14
+#define CU_DEVICE_ATTRIBUTE_GPU_OVERLAP 15
+#define CU_DEVICE_ATTRIBUTE_MULTIPROCESSOR_COUNT 16
+#define CU_DEVICE_ATTRIBUTE_KERNEL_EXEC_TIMEOUT 17
+#define CU_DEVICE_ATTRIBUTE_INTEGRATED 18
+#define CU_DEVICE_ATTRIBUTE_ECC_ENABLED 32
+#define CU_DEVICE_ATTRIBUTE_PCI_BUS_ID 33
+#define CU_DEVICE_ATTRIBUTE_PCI_DEVICE_ID 34
+#define CU_DEVICE_ATTRIBUTE_ASYNC_ENGINE_COUNT 40
+#define CU_DEVICE_ATTRIBUTE_PCI_DOMAIN_ID 50
+#define CU_DEVICE_ATTRIBUTE_COMPUTE_CAPABILITY_MAJOR 75
+#define CU_DEVICE_ATTRIBUTE_COMPUTE_CAPABILITY_MINOR 76
+#define CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_BLOCK 97
+#define CU_CTX_MAP_HOST 8
+#define CU_EVENT_DEFAULT 0
+#define CU_EVENT_DISABLE_TIMING 2
+#define CU_STREAM_WAIT_VALUE_GEQ 0
+#define CU_STREAM_NON_BLOCKING 1
+#define CU_MEMHOSTREGISTER_DEVICEMAP 2
+#define CU_MEMORYTYPE_HOST 1
+#define CU_MEMORYTYPE_DEVICE 2
+#define CU_MEMHOSTALLOC_DEVICEMAP 2
+#define CU_JIT_ERROR_LOG_BUFFER 5
+#define CU_JIT_ERROR_LOG_BUFFER_SIZE_BYTES 6
+CUresult cuCtxCreate(CUcontext *, unsigned int, CUdevice);
+CUresult cuCtxDestroy(CUcontext);
+CUresult cuCtxSetCurrent(CUcontext);
+CUresult cuDeviceGet(CUdevice *, int);
+CUresult cuDeviceGetAttribute(int *, CUdevice_attirbute, CUdevice);
+CUresult cuDeviceGetCount(int *);
+CUresult cuDeviceGetName(char *, int, CUdevice);
+CUresult cuEventCreate(CUevent *, unsigned int);
+CUresult cuEventDestroy(CUevent);
+CUresult cuEventElapsedTime(float *, CUevent, CUevent);
+CUresult cuEventRecord(CUevent, CUstream);
+CUresult cuEventSynchronize(CUevent);
+CUresult cuGetErrorName(CUresult error, const char **);
+CUresult cuGetErrorString(CUresult error, const char **);
+CUresult cuInit(int);
+CUresult cuLaunchKernel(CUfunction, unsigned int, unsigned int, unsigned int, unsigned int, unsigned int, unsigned int, unsigned int, CUstream, void **, void **);
+CUresult cuMemAlloc(CUdeviceptr *, size_t);
+CUresult cuMemcpy3DAsync(const CUDA_MEMCPY3D *, CUstream);
+CUresult cuMemcpyDtoDAsync(CUdeviceptr, CUdeviceptr, size_t, CUstream);
+CUresult cuMemcpyDtoH(void *, CUdeviceptr, size_t);
+CUresult cuMemcpyDtoHAsync(void *, CUdeviceptr, size_t, CUstream);
+CUresult cuMemcpyHtoD(CUdeviceptr, const void *, size_t);
+CUresult cuMemcpyHtoD(CUdeviceptr, const void *, size_t);
+CUresult cuMemcpyHtoDAsync(CUdeviceptr, const void *, unsigned int, CUstream);
+CUresult cuMemFree(CUdeviceptr);
+CUresult cuMemFreeHost(void *);
+CUresult cuMemGetInfo(size_t *, size_t *);
+CUresult cuMemHostAlloc(void **, size_t, unsigned int);
+CUresult cuMemHostGetDevicePointer(CUdeviceptr *, void *, unsigned int);
+CUresult cuMemHostRegister(void *, size_t, unsigned int);
+CUresult cuMemHostUnregister(void *);
+CUresult cuMemsetD16Async(CUdeviceptr, unsigned short, size_t, CUstream);
+CUresult cuMemsetD32Async(CUdeviceptr, unsigned int, size_t, CUstream);
+CUresult cuMemsetD8Async(CUdeviceptr, unsigned char, size_t, CUstream);
+CUresult cuModuleGetFunction(CUfunction *, CUmodule, const char *);
+CUresult cuModuleGetGlobal(CUdeviceptr *, size_t *, CUmodule, const char *);
+CUresult cuModuleLoadData(CUmodule *, const void *);
+CUresult cuModuleLoadDataEx(CUmodule *, const void *, unsigned int, CUjit_option *, void **);
+CUresult cuStreamCreate(CUstream *, unsigned int);
+CUresult cuStreamDestroy(CUstream);
+CUresult cuStreamSynchronize(CUstream);
+CUresult cuStreamWaitEvent(CUstream, CUevent, unsigned int);
+CUresult cuStreamWaitValue32(CUstream, CUdeviceptr, uint32_t, unsigned int);
+#endif /* _CUDA_H_ */
--- origsrc/pocl-3.1/lib/CL/devices/cuda/nvcuda.def 1970-01-01 09:00:00.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/cuda/nvcuda.def 2024-01-04 03:05:15.049153700 +0900
@@ -0,0 +1,657 @@
+;
+; Definition file of nvcuda_loader.dll
+; Automatic generated by gendef
+; written by Kai Tietz 2008
+;
+LIBRARY "nvcuda_loader.dll"
+EXPORTS
+cuArray3DCreate
+cuArray3DCreate_v2
+cuArray3DGetDescriptor
+cuArray3DGetDescriptor_v2
+cuArrayCreate
+cuArrayCreate_v2
+cuArrayDestroy
+cuArrayGetDescriptor
+cuArrayGetDescriptor_v2
+cuArrayGetMemoryRequirements
+cuArrayGetPlane
+cuArrayGetSparseProperties
+cuCoredumpGetAttribute
+cuCoredumpGetAttributeGlobal
+cuCoredumpSetAttribute
+cuCoredumpSetAttributeGlobal
+cuCtxAttach
+cuCtxCreate
+cuCtxCreate_v2
+cuCtxCreate_v3
+cuCtxDestroy
+cuCtxDestroy_v2
+cuCtxDetach
+cuCtxDisablePeerAccess
+cuCtxEnablePeerAccess
+cuCtxGetApiVersion
+cuCtxGetCacheConfig
+cuCtxGetCurrent
+cuCtxGetDevice
+cuCtxGetExecAffinity
+cuCtxGetFlags
+cuCtxGetId
+cuCtxGetLimit
+cuCtxGetSharedMemConfig
+cuCtxGetStreamPriorityRange
+cuCtxPopCurrent
+cuCtxPopCurrent_v2
+cuCtxPushCurrent
+cuCtxPushCurrent_v2
+cuCtxResetPersistingL2Cache
+cuCtxSetCacheConfig
+cuCtxSetCurrent
+cuCtxSetFlags
+cuCtxSetLimit
+cuCtxSetSharedMemConfig
+cuCtxSynchronize
+cuD3D10CtxCreate
+cuD3D10CtxCreateOnDevice
+cuD3D10CtxCreate_v2
+cuD3D10GetDevice
+cuD3D10GetDevices
+cuD3D10GetDirect3DDevice
+cuD3D10MapResources
+cuD3D10RegisterResource
+cuD3D10ResourceGetMappedArray
+cuD3D10ResourceGetMappedPitch
+cuD3D10ResourceGetMappedPitch_v2
+cuD3D10ResourceGetMappedPointer
+cuD3D10ResourceGetMappedPointer_v2
+cuD3D10ResourceGetMappedSize
+cuD3D10ResourceGetMappedSize_v2
+cuD3D10ResourceGetSurfaceDimensions
+cuD3D10ResourceGetSurfaceDimensions_v2
+cuD3D10ResourceSetMapFlags
+cuD3D10UnmapResources
+cuD3D10UnregisterResource
+cuD3D11CtxCreate
+cuD3D11CtxCreateOnDevice
+cuD3D11CtxCreate_v2
+cuD3D11GetDevice
+cuD3D11GetDevices
+cuD3D11GetDirect3DDevice
+cuD3D9Begin
+cuD3D9CtxCreate
+cuD3D9CtxCreateOnDevice
+cuD3D9CtxCreate_v2
+cuD3D9End
+cuD3D9GetDevice
+cuD3D9GetDevices
+cuD3D9GetDirect3DDevice
+cuD3D9MapResources
+cuD3D9MapVertexBuffer
+cuD3D9MapVertexBuffer_v2
+cuD3D9RegisterResource
+cuD3D9RegisterVertexBuffer
+cuD3D9ResourceGetMappedArray
+cuD3D9ResourceGetMappedPitch
+cuD3D9ResourceGetMappedPitch_v2
+cuD3D9ResourceGetMappedPointer
+cuD3D9ResourceGetMappedPointer_v2
+cuD3D9ResourceGetMappedSize
+cuD3D9ResourceGetMappedSize_v2
+cuD3D9ResourceGetSurfaceDimensions
+cuD3D9ResourceGetSurfaceDimensions_v2
+cuD3D9ResourceSetMapFlags
+cuD3D9UnmapResources
+cuD3D9UnmapVertexBuffer
+cuD3D9UnregisterResource
+cuD3D9UnregisterVertexBuffer
+cuDestroyExternalMemory
+cuDestroyExternalSemaphore
+cuDeviceCanAccessPeer
+cuDeviceComputeCapability
+cuDeviceGet
+cuDeviceGetAttribute
+cuDeviceGetByPCIBusId
+cuDeviceGetCount
+cuDeviceGetDefaultMemPool
+cuDeviceGetExecAffinitySupport
+cuDeviceGetGraphMemAttribute
+cuDeviceGetLuid
+cuDeviceGetMemPool
+cuDeviceGetName
+cuDeviceGetP2PAttribute
+cuDeviceGetPCIBusId
+cuDeviceGetProperties
+cuDeviceGetTexture1DLinearMaxWidth
+cuDeviceGetUuid
+cuDeviceGetUuid_v2
+cuDeviceGraphMemTrim
+cuDevicePrimaryCtxGetState
+cuDevicePrimaryCtxRelease
+cuDevicePrimaryCtxRelease_v2
+cuDevicePrimaryCtxReset
+cuDevicePrimaryCtxReset_v2
+cuDevicePrimaryCtxRetain
+cuDevicePrimaryCtxSetFlags
+cuDevicePrimaryCtxSetFlags_v2
+cuDeviceSetGraphMemAttribute
+cuDeviceSetMemPool
+cuDeviceTotalMem
+cuDeviceTotalMem_v2
+cuDriverGetVersion
+cuEventCreate
+cuEventDestroy
+cuEventDestroy_v2
+cuEventElapsedTime
+cuEventQuery
+cuEventRecord
+cuEventRecordWithFlags
+cuEventRecordWithFlags_ptsz
+cuEventRecord_ptsz
+cuEventSynchronize
+cuExternalMemoryGetMappedBuffer
+cuExternalMemoryGetMappedMipmappedArray
+cuFlushGPUDirectRDMAWrites
+cuFuncGetAttribute
+cuFuncGetModule
+cuFuncGetName
+cuFuncSetAttribute
+cuFuncSetBlockShape
+cuFuncSetCacheConfig
+cuFuncSetSharedMemConfig
+cuFuncSetSharedSize
+cuGLCtxCreate
+cuGLCtxCreate_v2
+cuGLGetDevices
+cuGLGetDevices_v2
+cuGLInit
+cuGLMapBufferObject
+cuGLMapBufferObjectAsync
+cuGLMapBufferObjectAsync_v2
+cuGLMapBufferObjectAsync_v2_ptsz
+cuGLMapBufferObject_v2
+cuGLMapBufferObject_v2_ptds
+cuGLRegisterBufferObject
+cuGLSetBufferObjectMapFlags
+cuGLUnmapBufferObject
+cuGLUnmapBufferObjectAsync
+cuGLUnregisterBufferObject
+cuGetErrorName
+cuGetErrorString
+cuGetExportTable
+cuGetProcAddress
+cuGetProcAddress_v2
+cuGraphAddBatchMemOpNode
+cuGraphAddChildGraphNode
+cuGraphAddDependencies
+cuGraphAddDependencies_v2
+cuGraphAddEmptyNode
+cuGraphAddEventRecordNode
+cuGraphAddEventWaitNode
+cuGraphAddExternalSemaphoresSignalNode
+cuGraphAddExternalSemaphoresWaitNode
+cuGraphAddHostNode
+cuGraphAddKernelNode
+cuGraphAddKernelNode_v2
+cuGraphAddMemAllocNode
+cuGraphAddMemFreeNode
+cuGraphAddMemcpyNode
+cuGraphAddMemsetNode
+cuGraphAddNode
+cuGraphAddNode_v2
+cuGraphBatchMemOpNodeGetParams
+cuGraphBatchMemOpNodeSetParams
+cuGraphChildGraphNodeGetGraph
+cuGraphClone
+cuGraphConditionalHandleCreate
+cuGraphCreate
+cuGraphDebugDotPrint
+cuGraphDestroy
+cuGraphDestroyNode
+cuGraphEventRecordNodeGetEvent
+cuGraphEventRecordNodeSetEvent
+cuGraphEventWaitNodeGetEvent
+cuGraphEventWaitNodeSetEvent
+cuGraphExecBatchMemOpNodeSetParams
+cuGraphExecChildGraphNodeSetParams
+cuGraphExecDestroy
+cuGraphExecEventRecordNodeSetEvent
+cuGraphExecEventWaitNodeSetEvent
+cuGraphExecExternalSemaphoresSignalNodeSetParams
+cuGraphExecExternalSemaphoresWaitNodeSetParams
+cuGraphExecGetFlags
+cuGraphExecHostNodeSetParams
+cuGraphExecKernelNodeSetParams
+cuGraphExecKernelNodeSetParams_v2
+cuGraphExecMemcpyNodeSetParams
+cuGraphExecMemsetNodeSetParams
+cuGraphExecNodeSetParams
+cuGraphExecUpdate
+cuGraphExecUpdate_v2
+cuGraphExternalSemaphoresSignalNodeGetParams
+cuGraphExternalSemaphoresSignalNodeSetParams
+cuGraphExternalSemaphoresWaitNodeGetParams
+cuGraphExternalSemaphoresWaitNodeSetParams
+cuGraphGetEdges
+cuGraphGetEdges_v2
+cuGraphGetNodes
+cuGraphGetRootNodes
+cuGraphHostNodeGetParams
+cuGraphHostNodeSetParams
+cuGraphInstantiate
+cuGraphInstantiateWithFlags
+cuGraphInstantiateWithParams
+cuGraphInstantiateWithParams_ptsz
+cuGraphInstantiate_v2
+cuGraphKernelNodeCopyAttributes
+cuGraphKernelNodeGetAttribute
+cuGraphKernelNodeGetParams
+cuGraphKernelNodeGetParams_v2
+cuGraphKernelNodeSetAttribute
+cuGraphKernelNodeSetParams
+cuGraphKernelNodeSetParams_v2
+cuGraphLaunch
+cuGraphLaunch_ptsz
+cuGraphMemAllocNodeGetParams
+cuGraphMemFreeNodeGetParams
+cuGraphMemcpyNodeGetParams
+cuGraphMemcpyNodeSetParams
+cuGraphMemsetNodeGetParams
+cuGraphMemsetNodeSetParams
+cuGraphNodeFindInClone
+cuGraphNodeGetDependencies
+cuGraphNodeGetDependencies_v2
+cuGraphNodeGetDependentNodes
+cuGraphNodeGetDependentNodes_v2
+cuGraphNodeGetEnabled
+cuGraphNodeGetType
+cuGraphNodeSetEnabled
+cuGraphNodeSetParams
+cuGraphReleaseUserObject
+cuGraphRemoveDependencies
+cuGraphRemoveDependencies_v2
+cuGraphRetainUserObject
+cuGraphUpload
+cuGraphUpload_ptsz
+cuGraphicsD3D10RegisterResource
+cuGraphicsD3D11RegisterResource
+cuGraphicsD3D9RegisterResource
+cuGraphicsGLRegisterBuffer
+cuGraphicsGLRegisterImage
+cuGraphicsMapResources
+cuGraphicsMapResources_ptsz
+cuGraphicsResourceGetMappedMipmappedArray
+cuGraphicsResourceGetMappedPointer
+cuGraphicsResourceGetMappedPointer_v2
+cuGraphicsResourceSetMapFlags
+cuGraphicsResourceSetMapFlags_v2
+cuGraphicsSubResourceGetMappedArray
+cuGraphicsUnmapResources
+cuGraphicsUnmapResources_ptsz
+cuGraphicsUnregisterResource
+cuImportExternalMemory
+cuImportExternalSemaphore
+cuInit
+cuIpcCloseMemHandle
+cuIpcGetEventHandle
+cuIpcGetMemHandle
+cuIpcOpenEventHandle
+cuIpcOpenMemHandle
+cuIpcOpenMemHandle_v2
+cuKernelGetAttribute
+cuKernelGetFunction
+cuKernelGetName
+cuKernelSetAttribute
+cuKernelSetCacheConfig
+cuLaunch
+cuLaunchCooperativeKernel
+cuLaunchCooperativeKernelMultiDevice
+cuLaunchCooperativeKernel_ptsz
+cuLaunchGrid
+cuLaunchGridAsync
+cuLaunchHostFunc
+cuLaunchHostFunc_ptsz
+cuLaunchKernel
+cuLaunchKernelEx
+cuLaunchKernelEx_ptsz
+cuLaunchKernel_ptsz
+cuLibraryGetGlobal
+cuLibraryGetKernel
+cuLibraryGetManaged
+cuLibraryGetModule
+cuLibraryGetUnifiedFunction
+cuLibraryLoadData
+cuLibraryLoadFromFile
+cuLibraryUnload
+cuLinkAddData
+cuLinkAddData_v2
+cuLinkAddFile
+cuLinkAddFile_v2
+cuLinkComplete
+cuLinkCreate
+cuLinkCreate_v2
+cuLinkDestroy
+cuMemAddressFree
+cuMemAddressReserve
+cuMemAdvise
+cuMemAdvise_v2
+cuMemAlloc
+cuMemAllocAsync
+cuMemAllocAsync_ptsz
+cuMemAllocFromPoolAsync
+cuMemAllocFromPoolAsync_ptsz
+cuMemAllocHost
+cuMemAllocHost_v2
+cuMemAllocManaged
+cuMemAllocPitch
+cuMemAllocPitch_v2
+cuMemAlloc_v2
+cuMemCreate
+cuMemExportToShareableHandle
+cuMemFree
+cuMemFreeAsync
+cuMemFreeAsync_ptsz
+cuMemFreeHost
+cuMemFree_v2
+cuMemGetAccess
+cuMemGetAddressRange
+cuMemGetAddressRange_v2
+cuMemGetAllocationGranularity
+cuMemGetAllocationPropertiesFromHandle
+cuMemGetHandleForAddressRange
+cuMemGetInfo
+cuMemGetInfo_v2
+cuMemHostAlloc
+cuMemHostGetDevicePointer
+cuMemHostGetDevicePointer_v2
+cuMemHostGetFlags
+cuMemHostRegister
+cuMemHostRegister_v2
+cuMemHostUnregister
+cuMemImportFromShareableHandle
+cuMemMap
+cuMemMapArrayAsync
+cuMemMapArrayAsync_ptsz
+cuMemPoolCreate
+cuMemPoolDestroy
+cuMemPoolExportPointer
+cuMemPoolExportToShareableHandle
+cuMemPoolGetAccess
+cuMemPoolGetAttribute
+cuMemPoolImportFromShareableHandle
+cuMemPoolImportPointer
+cuMemPoolSetAccess
+cuMemPoolSetAttribute
+cuMemPoolTrimTo
+cuMemPrefetchAsync
+cuMemPrefetchAsync_ptsz
+cuMemPrefetchAsync_v2
+cuMemPrefetchAsync_v2_ptsz
+cuMemRangeGetAttribute
+cuMemRangeGetAttributes
+cuMemRelease
+cuMemRetainAllocationHandle
+cuMemSetAccess
+cuMemUnmap
+cuMemcpy
+cuMemcpy2D
+cuMemcpy2DAsync
+cuMemcpy2DAsync_v2
+cuMemcpy2DAsync_v2_ptsz
+cuMemcpy2DUnaligned
+cuMemcpy2DUnaligned_v2
+cuMemcpy2DUnaligned_v2_ptds
+cuMemcpy2D_v2
+cuMemcpy2D_v2_ptds
+cuMemcpy3D
+cuMemcpy3DAsync
+cuMemcpy3DAsync_v2
+cuMemcpy3DAsync_v2_ptsz
+cuMemcpy3DPeer
+cuMemcpy3DPeerAsync
+cuMemcpy3DPeerAsync_ptsz
+cuMemcpy3DPeer_ptds
+cuMemcpy3D_v2
+cuMemcpy3D_v2_ptds
+cuMemcpyAsync
+cuMemcpyAsync_ptsz
+cuMemcpyAtoA
+cuMemcpyAtoA_v2
+cuMemcpyAtoA_v2_ptds
+cuMemcpyAtoD
+cuMemcpyAtoD_v2
+cuMemcpyAtoD_v2_ptds
+cuMemcpyAtoH
+cuMemcpyAtoHAsync
+cuMemcpyAtoHAsync_v2
+cuMemcpyAtoHAsync_v2_ptsz
+cuMemcpyAtoH_v2
+cuMemcpyAtoH_v2_ptds
+cuMemcpyDtoA
+cuMemcpyDtoA_v2
+cuMemcpyDtoA_v2_ptds
+cuMemcpyDtoD
+cuMemcpyDtoDAsync
+cuMemcpyDtoDAsync_v2
+cuMemcpyDtoDAsync_v2_ptsz
+cuMemcpyDtoD_v2
+cuMemcpyDtoD_v2_ptds
+cuMemcpyDtoH
+cuMemcpyDtoHAsync
+cuMemcpyDtoHAsync_v2
+cuMemcpyDtoHAsync_v2_ptsz
+cuMemcpyDtoH_v2
+cuMemcpyDtoH_v2_ptds
+cuMemcpyHtoA
+cuMemcpyHtoAAsync
+cuMemcpyHtoAAsync_v2
+cuMemcpyHtoAAsync_v2_ptsz
+cuMemcpyHtoA_v2
+cuMemcpyHtoA_v2_ptds
+cuMemcpyHtoD
+cuMemcpyHtoDAsync
+cuMemcpyHtoDAsync_v2
+cuMemcpyHtoDAsync_v2_ptsz
+cuMemcpyHtoD_v2
+cuMemcpyHtoD_v2_ptds
+cuMemcpyPeer
+cuMemcpyPeerAsync
+cuMemcpyPeerAsync_ptsz
+cuMemcpyPeer_ptds
+cuMemcpy_ptds
+cuMemsetD16
+cuMemsetD16Async
+cuMemsetD16Async_ptsz
+cuMemsetD16_v2
+cuMemsetD16_v2_ptds
+cuMemsetD2D16
+cuMemsetD2D16Async
+cuMemsetD2D16Async_ptsz
+cuMemsetD2D16_v2
+cuMemsetD2D16_v2_ptds
+cuMemsetD2D32
+cuMemsetD2D32Async
+cuMemsetD2D32Async_ptsz
+cuMemsetD2D32_v2
+cuMemsetD2D32_v2_ptds
+cuMemsetD2D8
+cuMemsetD2D8Async
+cuMemsetD2D8Async_ptsz
+cuMemsetD2D8_v2
+cuMemsetD2D8_v2_ptds
+cuMemsetD32
+cuMemsetD32Async
+cuMemsetD32Async_ptsz
+cuMemsetD32_v2
+cuMemsetD32_v2_ptds
+cuMemsetD8
+cuMemsetD8Async
+cuMemsetD8Async_ptsz
+cuMemsetD8_v2
+cuMemsetD8_v2_ptds
+cuMipmappedArrayCreate
+cuMipmappedArrayDestroy
+cuMipmappedArrayGetLevel
+cuMipmappedArrayGetMemoryRequirements
+cuMipmappedArrayGetSparseProperties
+cuModuleGetFunction
+cuModuleGetGlobal
+cuModuleGetGlobal_v2
+cuModuleGetLoadingMode
+cuModuleGetSurfRef
+cuModuleGetTexRef
+cuModuleLoad
+cuModuleLoadData
+cuModuleLoadDataEx
+cuModuleLoadFatBinary
+cuModuleUnload
+cuMulticastAddDevice
+cuMulticastBindAddr
+cuMulticastBindMem
+cuMulticastCreate
+cuMulticastGetGranularity
+cuMulticastUnbind
+cuOccupancyAvailableDynamicSMemPerBlock
+cuOccupancyMaxActiveBlocksPerMultiprocessor
+cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags
+cuOccupancyMaxActiveClusters
+cuOccupancyMaxPotentialBlockSize
+cuOccupancyMaxPotentialBlockSizeWithFlags
+cuOccupancyMaxPotentialClusterSize
+cuParamSetSize
+cuParamSetTexRef
+cuParamSetf
+cuParamSeti
+cuParamSetv
+cuPointerGetAttribute
+cuPointerGetAttributes
+cuPointerSetAttribute
+cuProfilerInitialize
+cuProfilerStart
+cuProfilerStop
+cuSignalExternalSemaphoresAsync
+cuSignalExternalSemaphoresAsync_ptsz
+cuStreamAddCallback
+cuStreamAddCallback_ptsz
+cuStreamAttachMemAsync
+cuStreamAttachMemAsync_ptsz
+cuStreamBatchMemOp
+cuStreamBatchMemOp_ptsz
+cuStreamBatchMemOp_v2
+cuStreamBatchMemOp_v2_ptsz
+cuStreamBeginCapture
+cuStreamBeginCaptureToGraph
+cuStreamBeginCaptureToGraph_ptsz
+cuStreamBeginCapture_ptsz
+cuStreamBeginCapture_v2
+cuStreamBeginCapture_v2_ptsz
+cuStreamCopyAttributes
+cuStreamCopyAttributes_ptsz
+cuStreamCreate
+cuStreamCreateWithPriority
+cuStreamDestroy
+cuStreamDestroy_v2
+cuStreamEndCapture
+cuStreamEndCapture_ptsz
+cuStreamGetAttribute
+cuStreamGetAttribute_ptsz
+cuStreamGetCaptureInfo
+cuStreamGetCaptureInfo_ptsz
+cuStreamGetCaptureInfo_v2
+cuStreamGetCaptureInfo_v2_ptsz
+cuStreamGetCaptureInfo_v3
+cuStreamGetCaptureInfo_v3_ptsz
+cuStreamGetCtx
+cuStreamGetCtx_ptsz
+cuStreamGetFlags
+cuStreamGetFlags_ptsz
+cuStreamGetId
+cuStreamGetId_ptsz
+cuStreamGetPriority
+cuStreamGetPriority_ptsz
+cuStreamIsCapturing
+cuStreamIsCapturing_ptsz
+cuStreamQuery
+cuStreamQuery_ptsz
+cuStreamSetAttribute
+cuStreamSetAttribute_ptsz
+cuStreamSynchronize
+cuStreamSynchronize_ptsz
+cuStreamUpdateCaptureDependencies
+cuStreamUpdateCaptureDependencies_ptsz
+cuStreamUpdateCaptureDependencies_v2
+cuStreamUpdateCaptureDependencies_v2_ptsz
+cuStreamWaitEvent
+cuStreamWaitEvent_ptsz
+cuStreamWaitValue32
+cuStreamWaitValue32_ptsz
+cuStreamWaitValue32_v2
+cuStreamWaitValue32_v2_ptsz
+cuStreamWaitValue64
+cuStreamWaitValue64_ptsz
+cuStreamWaitValue64_v2
+cuStreamWaitValue64_v2_ptsz
+cuStreamWriteValue32
+cuStreamWriteValue32_ptsz
+cuStreamWriteValue32_v2
+cuStreamWriteValue32_v2_ptsz
+cuStreamWriteValue64
+cuStreamWriteValue64_ptsz
+cuStreamWriteValue64_v2
+cuStreamWriteValue64_v2_ptsz
+cuSurfObjectCreate
+cuSurfObjectDestroy
+cuSurfObjectGetResourceDesc
+cuSurfRefGetArray
+cuSurfRefSetArray
+cuTensorMapEncodeIm2col
+cuTensorMapEncodeTiled
+cuTensorMapReplaceAddress
+cuTexObjectCreate
+cuTexObjectDestroy
+cuTexObjectGetResourceDesc
+cuTexObjectGetResourceViewDesc
+cuTexObjectGetTextureDesc
+cuTexRefCreate
+cuTexRefDestroy
+cuTexRefGetAddress
+cuTexRefGetAddressMode
+cuTexRefGetAddress_v2
+cuTexRefGetArray
+cuTexRefGetBorderColor
+cuTexRefGetFilterMode
+cuTexRefGetFlags
+cuTexRefGetFormat
+cuTexRefGetMaxAnisotropy
+cuTexRefGetMipmapFilterMode
+cuTexRefGetMipmapLevelBias
+cuTexRefGetMipmapLevelClamp
+cuTexRefGetMipmappedArray
+cuTexRefSetAddress
+cuTexRefSetAddress2D
+cuTexRefSetAddress2D_v2
+cuTexRefSetAddress2D_v3
+cuTexRefSetAddressMode
+cuTexRefSetAddress_v2
+cuTexRefSetArray
+cuTexRefSetBorderColor
+cuTexRefSetFilterMode
+cuTexRefSetFlags
+cuTexRefSetFormat
+cuTexRefSetMaxAnisotropy
+cuTexRefSetMipmapFilterMode
+cuTexRefSetMipmapLevelBias
+cuTexRefSetMipmapLevelClamp
+cuTexRefSetMipmappedArray
+cuThreadExchangeStreamCaptureMode
+cuUserObjectCreate
+cuUserObjectRelease
+cuUserObjectRetain
+cuWGLGetDevice
+cuWaitExternalSemaphoresAsync
+cuWaitExternalSemaphoresAsync_ptsz
+cudbgApiAttach
+cudbgApiDetach
+cudbgApiInit
+cudbgGetAPI
+cudbgGetAPIVersion
+cudbgMain
--- origsrc/pocl-3.1/lib/CL/devices/cuda/pocl-cuda.c 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/cuda/pocl-cuda.c 2024-01-04 03:05:15.052152000 +0900
@@ -47,8 +47,7 @@
#include <sys/stat.h>
#include <sys/types.h>
-#include <cuda.h>
-#include <cuda_runtime.h>
+#include "cuda.h"
#ifdef ENABLE_CUDNN
#include <cudnn.h>
@@ -73,6 +72,10 @@ cudnnHandle_t cudnn;
} \
}
+#ifdef __CYGWIN__
+#undef POCL_DEBUG_MESSAGES
+#endif
+
typedef struct pocl_cuda_device_data_s
{
CUdevice device;
@@ -2107,7 +2113,8 @@ pocl_cuda_free_event_data (cl_event even
{
pocl_cuda_event_data_t *event_data
= (pocl_cuda_event_data_t *)event->data;
- PTHREAD_CHECK (pthread_cond_destroy (&event_data->event_cond));
+ if (event_data->event_cond)
+ PTHREAD_CHECK (pthread_cond_destroy (&event_data->event_cond));
if (event->queue->properties & CL_QUEUE_PROFILING_ENABLE)
cuEventDestroy (event_data->start);
cuEventDestroy (event_data->end);
--- origsrc/pocl-3.1/lib/CL/devices/cuda/pocl-ptx-gen.cc 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/cuda/pocl-ptx-gen.cc 2024-01-04 03:18:37.421667500 +0900
@@ -555,8 +555,9 @@ int findLibDevice(char LibDevicePath[PAT
LibDeviceSM = 30;
const char *BasePath[] = {
- pocl_get_string_option("POCL_CUDA_TOOLKIT_PATH", CUDA_TOOLKIT_ROOT_DIR),
+ pocl_get_string_option("POCL_CUDA_TOOLKIT_PATH", "/usr/local/cuda"),
pocl_get_string_option("CUDA_HOME", "/usr/local/cuda"),
+ pocl_get_string_option("CUDA_PATH", "/usr/local/cuda"),
"/usr/local/lib/cuda",
"/usr/local/lib",
"/usr/lib",
@@ -613,7 +614,7 @@ void linkLibDevice(llvm::Module *Module,
const char *LibDevicePath) {
auto Buffer = llvm::MemoryBuffer::getFile(LibDevicePath);
if (!Buffer)
- POCL_ABORT("[CUDA] failed to open libdevice library file\n");
+ POCL_ABORT("[CUDA] failed to open libdevice library file. Most likely, you do not have NVIDIA CUDA Toolkit. Please consider to install it. If you have it installed, set CUDA_PATH properly.\n");
POCL_MSG_PRINT_INFO("loading libdevice from '%s'\n", LibDevicePath);
@@ -960,11 +961,19 @@ int pocl_cuda_get_ptr_arg_alignment(cons
llvm::dyn_cast<llvm::GetElementPtrInst>(U)) {
for (auto UU : GEP->users()) {
if (llvm::StoreInst *SI = llvm::dyn_cast<llvm::StoreInst>(UU)) {
+#ifdef LLVM_OLDER_THAN_15_0
+ Alignments[i] = SI->getAlignment();
+#else
Alignments[i] = SI->getAlign().value();
+#endif
break;
}
if (llvm::LoadInst *LI = llvm::dyn_cast<llvm::LoadInst>(UU)) {
+#ifdef LLVM_OLDER_THAN_15_0
+ Alignments[i] = LI->getAlignment();
+#else
Alignments[i] = LI->getAlign().value();
+#endif
break;
}
}
--- origsrc/pocl-3.1/lib/CL/devices/topology/pocl_topology.c 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/devices/topology/pocl_topology.c 2024-01-04 03:05:15.058148600 +0900
@@ -205,7 +205,7 @@ exit_destroy:
}
// #ifdef HWLOC
-#elif defined(__linux__) || defined(__ANDROID__)
+#elif defined(__linux__) || defined(__ANDROID__) || defined(__CYGWIN__)
#define L3_CACHE_SIZE "/sys/devices/system/cpu/cpu0/cache/index3/size"
#define L2_CACHE_SIZE "/sys/devices/system/cpu/cpu0/cache/index2/size"
--- origsrc/pocl-3.1/lib/CL/pocl_build.c 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/pocl_build.c 2024-01-04 03:05:15.061147000 +0900
@@ -690,6 +690,13 @@ compile_and_link_program(int compile_pro
goto ERROR_CLEAN_OPTIONS;
}
+#ifdef __CYGWIN__
+ if (program->compiler_options == NULL)
+ {
+ program->compiler_options = (char *)malloc(512);
+ program->compiler_options[0] = '\0';
+ }
+#endif
POCL_MSG_PRINT_LLVM ("building program with options %s\n",
program->compiler_options);
--- origsrc/pocl-3.1/lib/CL/pocl_util.c 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/CL/pocl_util.c 2024-01-04 03:05:15.064145100 +0900
@@ -59,8 +59,10 @@
#if defined(__APPLE__)
#define _DARWIN_C_SOURCE
#endif
-#ifdef __linux__
+#if defined(__linux__) || defined(__CYGWIN__)
#define _GNU_SOURCE
+#undef __GNU_VISIBLE
+#define __GNU_VISIBLE 1
#endif
#include <dlfcn.h>
#endif
--- origsrc/pocl-3.1/lib/kernel/host/spir_wrapper32.ll 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/kernel/host/spir_wrapper32.ll 2024-01-04 03:05:15.066143900 +0900
@@ -2663,7 +2663,7 @@ attributes #0 = { nounwind "correctly-ro
!0 = !{i32 1, i32 2}
!1 = !{!"clang version 6.0.0"}
-!2 = !{i32 1, !"wchar_size", i32 4}
+!2 = !{i32 1, !"wchar_size", i32 2}
!3 = !{i32 7, !"PIC Level", i32 2}
--- origsrc/pocl-3.1/lib/kernel/host/spir_wrapper64.ll 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/kernel/host/spir_wrapper64.ll 2024-01-04 03:05:15.071141100 +0900
@@ -14731,7 +14731,7 @@ attributes #0 = { nounwind "correctly-ro
!0 = !{i32 1, i32 2}
!1 = !{!"clang version 6.0.0"}
-!2 = !{i32 1, !"wchar_size", i32 4}
+!2 = !{i32 1, !"wchar_size", i32 2}
!3 = !{i32 7, !"PIC Level", i32 2}
--- origsrc/pocl-3.1/lib/llvmopencl/CMakeLists.txt 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/llvmopencl/CMakeLists.txt 2024-01-04 03:05:15.075138700 +0900
@@ -115,9 +115,10 @@ harden("llvmopencl")
# not sure where other platforms get their library linkage list, probably there is
# way to make this more consistent on different platforms
-if(MSVC)
+if(WIN32 OR CYGWIN)
+ target_link_libraries("llvmopencl" pocl)
target_link_libraries("llvmopencl" ${POCL_LLVM_LIBS})
-endif(MSVC)
+endif(WIN32 OR CYGWIN)
#target_link_libraries("llvmopencl" "${LLVM_SYSLIBS}")
endif(ENABLE_LIBLLVMOPENCL)
--- origsrc/pocl-3.1/lib/llvmopencl/DebugHelpers.h 2022-12-05 21:36:08.000000000 +0900
+++ src/pocl-3.1/lib/llvmopencl/DebugHelpers.h 2024-01-04 03:05:15.077137600 +0900
@@ -24,7 +24,7 @@
#define _POCL_DEBUG_HELPERS_H
#include <string>
-#if _MSC_VER
+#if _MSC_VER || defined(__CYGWIN__)
# include <set>
#endif
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 9:29 ` Takashi Yano
2024-01-03 11:38 ` Brian Inglis
@ 2024-01-07 12:51 ` Jon Turney
2024-01-07 13:05 ` Takashi Yano
1 sibling, 1 reply; 18+ messages in thread
From: Jon Turney @ 2024-01-07 12:51 UTC (permalink / raw)
To: Takashi Yano; +Cc: cygwin-apps
On 03/01/2024 09:29, Takashi Yano via Cygwin-apps wrote:
>>>
>>>> - Enable CUDA support.
>>
>> Curiosity, how do we support CUDA on Cygwin ?
>
> nvidia cuda toolkit is used in build stage of user programs.
> Although this is not very desirable for cygwin package, I thought
> that the advantage of being able to use the GPU was greater than
> the disadvantage.
>
> However, on the second thought, cuda support should be a separeted
> package from the base package, and suggest installing cuda toolkit
> in the install stage of of that package.
If a 3rd party driver etc. needs to be installed for a Cygwin package to
work, we have in the past used the 'message' line in a .hint so setup
says that when it is installed.
(Unfortunately, generating that line is not currently supported by
cygport, I think)
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-07 12:51 ` Jon Turney
@ 2024-01-07 13:05 ` Takashi Yano
0 siblings, 0 replies; 18+ messages in thread
From: Takashi Yano @ 2024-01-07 13:05 UTC (permalink / raw)
To: cygwin-apps
On Sun, 7 Jan 2024 12:51:42 +0000
Jon Turney wrote:
> On 03/01/2024 09:29, Takashi Yano via Cygwin-apps wrote:
> >>>
> >>>> - Enable CUDA support.
> >>
> >> Curiosity, how do we support CUDA on Cygwin ?
> >
> > nvidia cuda toolkit is used in build stage of user programs.
> > Although this is not very desirable for cygwin package, I thought
> > that the advantage of being able to use the GPU was greater than
> > the disadvantage.
> >
> > However, on the second thought, cuda support should be a separeted
> > package from the base package, and suggest installing cuda toolkit
> > in the install stage of of that package.
>
> If a 3rd party driver etc. needs to be installed for a Cygwin package to
> work, we have in the past used the 'message' line in a .hint so setup
> says that when it is installed.
>
> (Unfortunately, generating that line is not currently supported by
> cygport, I think)
Thanks for the advice.
In the latest release candidate, cuda suppourt module is not
in separated package. Instead, if NVIDIA GPU is detected and
user specify to use GPU, but CUDA Toolkit is not installed:
On Thu, 4 Jan 2024 09:55:07 +0900
Takashi Yano wrote:
> time to build the kernel objects. If no CUDA Toolkit is found at
> this time, the message:
> "[CUDA] failed to open libdevice library file. Most likely, you do
> not have NVIDIA CUDA Toolkit. Please consider to install it. If you
> have it installed, set CUDA_PATH properly."
> will be shown.
--
Takashi Yano <takashi.yano@nifty.ne.jp>
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-03 7:54 ` Marco Atzeri
2024-01-03 9:29 ` Takashi Yano
@ 2024-01-08 0:38 ` Andrew Schulman
1 sibling, 0 replies; 18+ messages in thread
From: Andrew Schulman @ 2024-01-08 0:38 UTC (permalink / raw)
To: cygwin-apps
> On 03/01/2024 06:25, Takashi Yano via Cygwin-apps wrote:
> > On Wed, 3 Jan 2024 14:14:12 +0900
> > Takashi Yano via Cygwin-apps <cygwin-apps@cygwin.com> wrote:
> >> I'd like to adopt the pocl package.
> >>
> >> - Update to latest upstream release.
>
> $ git diff |grep "^+"
> +++ b/cygwin-pkg-maint
> +pocl Takashi Yano
Gold star awarded! https://cygwin.com/goldstars/#TY
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-04 0:55 ` Takashi Yano
@ 2024-01-13 15:48 ` Jon Turney
2024-01-14 14:57 ` Takashi Yano
0 siblings, 1 reply; 18+ messages in thread
From: Jon Turney @ 2024-01-13 15:48 UTC (permalink / raw)
To: Takashi Yano; +Cc: cygwin-apps
On 04/01/2024 00:55, Takashi Yano via Cygwin-apps wrote:
[...]
> Any comments and advices will be appreciated.
Thanks for adopting this.
> pocl.cygport
>
> inherit clang cmake
>
> NAME="pocl"
> VERSION=3.1
> RELEASE=1
> CATEGORY="Libs"
> # The entire code is under MIT
> # include/utlist.h which is under BSD-1-Clause (unbundled)
> # lib/kernel/vecmath which is under GPL-3.0-or-later OR LGPL-3.0-or-later
> LICENSE="MIT, BSD-1-Clause, GPL-3.0-or-later OR LGPL-3.0-or-later"
I think this is going to fail to validate as an SPDX license expression.
The identifiers should be combined with AND and OR (where OR represents
a choice, and AND represents compliance with both alternatives is required).
When I try to build it fails:
[449/761] Linking CXX shared module lib/llvmopencl/cygllvmopencl.dll
FAILED: lib/llvmopencl/cygllvmopencl.dll
[...]
/usr/bin/ld: cannot find -lpocl: No such file or directory
clang-8: error: linker command failed with exit code 1 (use -v to see
invocation)
I don't know if that means it's looking for the installed rather than
just built libpocl there, or something else is wrong.
Otherwise, looks good.
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-13 15:48 ` Jon Turney
@ 2024-01-14 14:57 ` Takashi Yano
2024-01-14 20:46 ` Jon Turney
0 siblings, 1 reply; 18+ messages in thread
From: Takashi Yano @ 2024-01-14 14:57 UTC (permalink / raw)
To: cygwin-apps
Hi Jon,
Thanks for revewing.
On Sat, 13 Jan 2024 15:48:33 +0000
Jon Turney wrote:
> On 04/01/2024 00:55, Takashi Yano via Cygwin-apps wrote:
> [...]
> > Any comments and advices will be appreciated.
>
> Thanks for adopting this.
>
> > pocl.cygport
> >
> > inherit clang cmake
> >
> > NAME="pocl"
> > VERSION=3.1
> > RELEASE=1
> > CATEGORY="Libs"
> > # The entire code is under MIT
> > # include/utlist.h which is under BSD-1-Clause (unbundled)
> > # lib/kernel/vecmath which is under GPL-3.0-or-later OR LGPL-3.0-or-later
> > LICENSE="MIT, BSD-1-Clause, GPL-3.0-or-later OR LGPL-3.0-or-later"
>
> I think this is going to fail to validate as an SPDX license expression.
> The identifiers should be combined with AND and OR (where OR represents
> a choice, and AND represents compliance with both alternatives is required).
What about "MIT AND BSD-1-Clause AND (GPL-3.0-or-later OR LGPL-3.0-or-later)"?
Is "()" allowed?
> When I try to build it fails:
>
> [449/761] Linking CXX shared module lib/llvmopencl/cygllvmopencl.dll
> FAILED: lib/llvmopencl/cygllvmopencl.dll
> [...]
> /usr/bin/ld: cannot find -lpocl: No such file or directory
> clang-8: error: linker command failed with exit code 1 (use -v to see
> invocation)
>
> I don't know if that means it's looking for the installed rather than
> just built libpocl there, or something else is wrong.
I cannot reproduce this even if I uninstall libpocl-devel. Umm, what
is the difference?
My environment is as follows.
Cygwin Package Information
Package Version Status
binutils 2.41-3 OK
clang 8.0.1-1 OK
cmake 3.25.3-1 OK
cygport 0.36.7-1 OK
ninja 1.11.1-1 OK
--
Takashi Yano <takashi.yano@nifty.ne.jp>
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-14 14:57 ` Takashi Yano
@ 2024-01-14 20:46 ` Jon Turney
2024-01-15 3:14 ` Takashi Yano
0 siblings, 1 reply; 18+ messages in thread
From: Jon Turney @ 2024-01-14 20:46 UTC (permalink / raw)
To: Takashi Yano; +Cc: cygwin-apps
On 14/01/2024 14:57, Takashi Yano via Cygwin-apps wrote:
> On Sat, 13 Jan 2024 15:48:33 +0000
> Jon Turney wrote:
>> On 04/01/2024 00:55, Takashi Yano via Cygwin-apps wrote:
>> [...]
>>> # The entire code is under MIT
>>> # include/utlist.h which is under BSD-1-Clause (unbundled)
>>> # lib/kernel/vecmath which is under GPL-3.0-or-later OR LGPL-3.0-or-later
>>> LICENSE="MIT, BSD-1-Clause, GPL-3.0-or-later OR LGPL-3.0-or-later"
>>
>> I think this is going to fail to validate as an SPDX license expression.
>> The identifiers should be combined with AND and OR (where OR represents
>> a choice, and AND represents compliance with both alternatives is required).
>
> What about "MIT AND BSD-1-Clause AND (GPL-3.0-or-later OR LGPL-3.0-or-later)"?
> Is "()" allowed?
Yes.
https://spdx.github.io/spdx-spec/v2-draft/SPDX-license-expressions/#d45-order-of-precedence-and-parentheses
>
>> When I try to build it fails:
>>
>> [449/761] Linking CXX shared module lib/llvmopencl/cygllvmopencl.dll
>> FAILED: lib/llvmopencl/cygllvmopencl.dll
>> [...]
>> /usr/bin/ld: cannot find -lpocl: No such file or directory
>> clang-8: error: linker command failed with exit code 1 (use -v to see
>> invocation)
>>
>> I don't know if that means it's looking for the installed rather than
>> just built libpocl there, or something else is wrong.
>
> I cannot reproduce this even if I uninstall libpocl-devel. Umm, what
> is the difference?
Yeah, confusing. I think it might have been caused by not having
libOpenCL-devel installed.
Anyhow, I can build it OK now, so all is good.
Maybe consider adding BUILD_REQUIRES="clang libllvm-devel libhwloc-devel
libOpenCL-devel ninja" or whatever is correct :)
^ permalink raw reply [flat|nested] 18+ messages in thread
* Re: [ITA] pocl
2024-01-14 20:46 ` Jon Turney
@ 2024-01-15 3:14 ` Takashi Yano
0 siblings, 0 replies; 18+ messages in thread
From: Takashi Yano @ 2024-01-15 3:14 UTC (permalink / raw)
To: cygwin-apps
On Sun, 14 Jan 2024 20:46:10 +0000
Jon Turney wrote:
> On 14/01/2024 14:57, Takashi Yano via Cygwin-apps wrote:
> > I cannot reproduce this even if I uninstall libpocl-devel. Umm, what
> > is the difference?
>
> Yeah, confusing. I think it might have been caused by not having
> libOpenCL-devel installed.
I could reproduce the same error by uninstalling libOpenCL-devel.
I guess libpocl.a/libpocl.dll.a failed to be built due to lack of
libOpenCL.a
> Anyhow, I can build it OK now, so all is good.
>
> Maybe consider adding BUILD_REQUIRES="clang libllvm-devel libhwloc-devel
> libOpenCL-devel ninja" or whatever is correct :)
Added:
BUILD_REQUIRES="cmake ninja libOpenCL-devel libhwloc-devel libclang-devel libllvm-devel"
--
Takashi Yano <takashi.yano@nifty.ne.jp>
^ permalink raw reply [flat|nested] 18+ messages in thread
end of thread, other threads:[~2024-01-15 3:14 UTC | newest]
Thread overview: 18+ messages (download: mbox.gz / follow: Atom feed)
-- links below jump to the message on this page --
2024-01-03 5:14 [ITA] pocl Takashi Yano
2024-01-03 5:25 ` Takashi Yano
2024-01-03 7:54 ` Marco Atzeri
2024-01-03 9:29 ` Takashi Yano
2024-01-03 11:38 ` Brian Inglis
2024-01-03 12:00 ` Takashi Yano
2024-01-03 12:26 ` Brian Inglis
2024-01-03 12:42 ` Takashi Yano
2024-01-03 12:30 ` Takashi Yano
2024-01-03 14:08 ` Takashi Yano
2024-01-04 0:55 ` Takashi Yano
2024-01-13 15:48 ` Jon Turney
2024-01-14 14:57 ` Takashi Yano
2024-01-14 20:46 ` Jon Turney
2024-01-15 3:14 ` Takashi Yano
2024-01-07 12:51 ` Jon Turney
2024-01-07 13:05 ` Takashi Yano
2024-01-08 0:38 ` Andrew Schulman
This is a public inbox, see mirroring instructions
for how to clone and mirror all data and code used for this inbox;
as well as URLs for read-only IMAP folder(s) and NNTP newsgroup(s).