1158fe4340
OpenMP 5.2 changed once more what device numbers are allowed. In 5.1, valid device numbers were [0, omp_get_num_devices()]. 5.2 makes also -1 valid (calls it omp_initial_device), which is equivalent in behavior to omp_get_num_devices() number but has the advantage that it is a constant. And it also introduces omp_invalid_device which is also a constant with implementation defined value < -1. That value should act like sNaN, any time any device construct (GOMP_target*) or OpenMP runtime API routine is asked for such a device, the program is terminated. And if OMP_TARGET_OFFLOAD=mandatory, all non-conforming device numbers (which is all but [-1, omp_get_num_devices()] other than omp_invalid_device) must be treated like omp_invalid_device. For device constructs, we have a compatibility problem, we've historically used 2 magic negative values to mean something special. GOMP_DEVICE_ICV (-1) means device clause wasn't present, pick the omp_get_default_device () number GOMP_DEVICE_FALLBACK (-2) means the host device (this is used e.g. for #pragma omp target if (cond) where if cond is false, we pass -2 But 5.2 requires that omp_initial_device is -1 (there were discussions about it, advantage of -1 is that one can say iterate over the [-1, omp_get_num_devices()-1] range to get all devices starting with the host/initial one. And also, if user passes -2, unless it is omp_invalid_device, we need to treat it like non-conforming with OMP_TARGET_OFFLOAD=mandatory. So, the patch does on the compiler side some number remapping, user_device_num >= -2U ? user_device_num - 1 : user_device_num. This remapping is done at compile time if device clause has constant argument, otherwise at runtime, and means that for user -1 (omp_initial_device) we pass -2 to GOMP_* in the runtime library where it treats it like host fallback, while -2 is remapped to -3 (one of the non-conforming device numbers, for those it doesn't matter which one is which). omp_invalid_device is then -4. For the OpenMP device runtime APIs, no remapping is done. This patch doesn't deal with the initial default-device-var for OMP_TARGET_OFFLOAD=mandatory , the spec says that the inital ICV value for that should in that case depend on whether there are any offloading devices or not (if not, should be omp_invalid_device), but that means we can't determine the number of devices lazily (and let libraries have the possibility to register their offloading data etc.). 2022-06-13 Jakub Jelinek <jakub@redhat.com> gcc/ * omp-expand.cc (expand_omp_target): Remap user provided device clause arguments, -1 to -2 and -2 to -3, either at compile time if constant, or at runtime. include/ * gomp-constants.h (GOMP_DEVICE_INVALID): Define. libgomp/ * omp.h.in (omp_initial_device, omp_invalid_device): New enumerators. * omp_lib.f90.in (omp_initial_device, omp_invalid_device): New parameters. * omp_lib.h.in (omp_initial_device, omp_invalid_device): Likewise. * target.c (resolve_device): Add remapped argument, handle GOMP_DEVICE_ICV only if remapped is true (and clear remapped), for negative values, treat GOMP_DEVICE_FALLBACK as fallback only if remapped, otherwise treat omp_initial_device that way. For omp_invalid_device, always emit gomp_fatal, even when OMP_TARGET_OFFLOAD isn't mandatory. (GOMP_target, GOMP_target_ext, GOMP_target_data, GOMP_target_data_ext, GOMP_target_update, GOMP_target_update_ext, GOMP_target_enter_exit_data): Pass true as remapped argument to resolve_device. (omp_target_alloc, omp_target_free, omp_target_is_present, omp_target_memcpy_check, omp_target_associate_ptr, omp_target_disassociate_ptr, omp_get_mapped_ptr, omp_target_is_accessible): Pass false as remapped argument to resolve_device. Treat omp_initial_device the same as gomp_get_num_devices (). Don't bypass resolve_device calls if device_num is negative. (omp_pause_resource): Treat omp_initial_device the same as gomp_get_num_devices (). Call resolve_device. * icv-device.c (omp_set_default_device): Always set to device_num even when it is negative. * libgomp.texi: Document that Conforming device numbers, omp_initial_device and omp_invalid_device is implemented. * testsuite/libgomp.c/target-41.c (main): Add test with omp_initial_device. * testsuite/libgomp.c/target-45.c: New test. * testsuite/libgomp.c/target-46.c: New test. * testsuite/libgomp.c/target-47.c: New test. * testsuite/libgomp.c-c++-common/target-is-accessible-1.c (main): Add test with omp_initial_device. Use -5 instead of -1 for negative value test. * testsuite/libgomp.fortran/target-is-accessible-1.f90 (main): Likewise. Reorder stop numbers.
483 lines
21 KiB
C
483 lines
21 KiB
C
! Copyright (C) 2005-2022 Free Software Foundation, Inc.
|
|
! Contributed by Jakub Jelinek <jakub@redhat.com>.
|
|
|
|
! This file is part of the GNU Offloading and Multi Processing Library
|
|
! (libgomp).
|
|
|
|
! Libgomp is free software; you can redistribute it and/or modify it
|
|
! under the terms of the GNU General Public License as published by
|
|
! the Free Software Foundation; either version 3, or (at your option)
|
|
! any later version.
|
|
|
|
! Libgomp is distributed in the hope that it will be useful, but WITHOUT ANY
|
|
! WARRANTY; without even the implied warranty of MERCHANTABILITY or FITNESS
|
|
! FOR A PARTICULAR PURPOSE. See the GNU General Public License for
|
|
! more details.
|
|
|
|
! Under Section 7 of GPL version 3, you are granted additional
|
|
! permissions described in the GCC Runtime Library Exception, version
|
|
! 3.1, as published by the Free Software Foundation.
|
|
|
|
! You should have received a copy of the GNU General Public License and
|
|
! a copy of the GCC Runtime Library Exception along with this program;
|
|
! see the files COPYING3 and COPYING.RUNTIME respectively. If not, see
|
|
! <http://www.gnu.org/licenses/>.
|
|
|
|
integer omp_lock_kind, omp_nest_lock_kind, openmp_version
|
|
parameter (omp_lock_kind = @OMP_LOCK_KIND@)
|
|
parameter (omp_nest_lock_kind = @OMP_NEST_LOCK_KIND@)
|
|
integer omp_depend_kind
|
|
parameter (omp_depend_kind = @OMP_DEPEND_KIND@)
|
|
integer omp_sched_kind
|
|
parameter (omp_sched_kind = 4)
|
|
integer (omp_sched_kind) omp_sched_static, omp_sched_dynamic
|
|
integer (omp_sched_kind) omp_sched_guided, omp_sched_auto
|
|
parameter (omp_sched_static = 1)
|
|
parameter (omp_sched_dynamic = 2)
|
|
parameter (omp_sched_guided = 3)
|
|
parameter (omp_sched_auto = 4)
|
|
integer omp_proc_bind_kind
|
|
parameter (omp_proc_bind_kind = 4)
|
|
integer (omp_proc_bind_kind) omp_proc_bind_false
|
|
integer (omp_proc_bind_kind) omp_proc_bind_true
|
|
integer (omp_proc_bind_kind) omp_proc_bind_primary
|
|
integer (omp_proc_bind_kind) omp_proc_bind_master
|
|
integer (omp_proc_bind_kind) omp_proc_bind_close
|
|
integer (omp_proc_bind_kind) omp_proc_bind_spread
|
|
parameter (omp_proc_bind_false = 0)
|
|
parameter (omp_proc_bind_true = 1)
|
|
parameter (omp_proc_bind_primary = 2)
|
|
parameter (omp_proc_bind_master = 2)
|
|
parameter (omp_proc_bind_close = 3)
|
|
parameter (omp_proc_bind_spread = 4)
|
|
integer omp_sync_hint_kind
|
|
integer omp_lock_hint_kind
|
|
parameter (omp_sync_hint_kind = 4)
|
|
parameter (omp_lock_hint_kind = omp_sync_hint_kind)
|
|
integer (omp_sync_hint_kind) omp_sync_hint_none
|
|
integer (omp_lock_hint_kind) omp_lock_hint_none
|
|
integer (omp_sync_hint_kind) omp_sync_hint_uncontended
|
|
integer (omp_lock_hint_kind) omp_lock_hint_uncontended
|
|
integer (omp_sync_hint_kind) omp_sync_hint_contended
|
|
integer (omp_sync_hint_kind) omp_lock_hint_contended
|
|
integer (omp_lock_hint_kind) omp_sync_hint_nonspeculative
|
|
integer (omp_lock_hint_kind) omp_lock_hint_nonspeculative
|
|
integer (omp_sync_hint_kind) omp_sync_hint_speculative
|
|
integer (omp_lock_hint_kind) omp_lock_hint_speculative
|
|
parameter (omp_sync_hint_none = 0)
|
|
parameter (omp_lock_hint_none = 0)
|
|
parameter (omp_sync_hint_uncontended = 1)
|
|
parameter (omp_lock_hint_uncontended = 1)
|
|
parameter (omp_sync_hint_contended = 2)
|
|
parameter (omp_lock_hint_contended = 2)
|
|
parameter (omp_sync_hint_nonspeculative = 4)
|
|
parameter (omp_lock_hint_nonspeculative = 4)
|
|
parameter (omp_sync_hint_speculative = 8)
|
|
parameter (omp_lock_hint_speculative = 8)
|
|
parameter (openmp_version = 201511)
|
|
integer omp_pause_resource_kind
|
|
parameter (omp_pause_resource_kind = 4)
|
|
integer (omp_pause_resource_kind) omp_pause_soft
|
|
integer (omp_pause_resource_kind) omp_pause_hard
|
|
parameter (omp_pause_soft = 1)
|
|
parameter (omp_pause_hard = 2)
|
|
|
|
integer omp_allocator_handle_kind, omp_alloctrait_key_kind
|
|
integer omp_alloctrait_val_kind, omp_memspace_handle_kind
|
|
integer omp_event_handle_kind
|
|
parameter (omp_allocator_handle_kind = @INTPTR_T_KIND@)
|
|
parameter (omp_alloctrait_key_kind = 4)
|
|
parameter (omp_alloctrait_val_kind = @INTPTR_T_KIND@)
|
|
parameter (omp_memspace_handle_kind = @INTPTR_T_KIND@)
|
|
parameter (omp_event_handle_kind = @INTPTR_T_KIND@)
|
|
integer (omp_alloctrait_key_kind) omp_atk_sync_hint
|
|
integer (omp_alloctrait_key_kind) omp_atk_alignment
|
|
integer (omp_alloctrait_key_kind) omp_atk_access
|
|
integer (omp_alloctrait_key_kind) omp_atk_pool_size
|
|
integer (omp_alloctrait_key_kind) omp_atk_fallback
|
|
integer (omp_alloctrait_key_kind) omp_atk_fb_data
|
|
integer (omp_alloctrait_key_kind) omp_atk_pinned
|
|
integer (omp_alloctrait_key_kind) omp_atk_partition
|
|
parameter (omp_atk_sync_hint = 1)
|
|
parameter (omp_atk_alignment = 2)
|
|
parameter (omp_atk_access = 3)
|
|
parameter (omp_atk_pool_size = 4)
|
|
parameter (omp_atk_fallback = 5)
|
|
parameter (omp_atk_fb_data = 6)
|
|
parameter (omp_atk_pinned = 7)
|
|
parameter (omp_atk_partition = 8)
|
|
integer (omp_alloctrait_val_kind) omp_atv_false
|
|
integer (omp_alloctrait_val_kind) omp_atv_true
|
|
integer (omp_alloctrait_val_kind) omp_atv_default
|
|
integer (omp_alloctrait_val_kind) omp_atv_contended
|
|
integer (omp_alloctrait_val_kind) omp_atv_uncontended
|
|
integer (omp_alloctrait_val_kind) omp_atv_serialized
|
|
integer (omp_alloctrait_val_kind) omp_atv_sequential
|
|
integer (omp_alloctrait_val_kind) omp_atv_private
|
|
integer (omp_alloctrait_val_kind) omp_atv_all
|
|
integer (omp_alloctrait_val_kind) omp_atv_thread
|
|
integer (omp_alloctrait_val_kind) omp_atv_pteam
|
|
integer (omp_alloctrait_val_kind) omp_atv_cgroup
|
|
integer (omp_alloctrait_val_kind) omp_atv_default_mem_fb
|
|
integer (omp_alloctrait_val_kind) omp_atv_null_fb
|
|
integer (omp_alloctrait_val_kind) omp_atv_abort_fb
|
|
integer (omp_alloctrait_val_kind) omp_atv_allocator_fb
|
|
integer (omp_alloctrait_val_kind) omp_atv_environment
|
|
integer (omp_alloctrait_val_kind) omp_atv_nearest
|
|
integer (omp_alloctrait_val_kind) omp_atv_blocked
|
|
integer (omp_alloctrait_val_kind) omp_atv_interleaved
|
|
parameter (omp_atv_default = -1)
|
|
parameter (omp_atv_false = 0)
|
|
parameter (omp_atv_true = 1)
|
|
parameter (omp_atv_contended = 3)
|
|
parameter (omp_atv_uncontended = 4)
|
|
parameter (omp_atv_serialized = 5)
|
|
parameter (omp_atv_sequential = omp_atv_serialized)
|
|
parameter (omp_atv_private = 6)
|
|
parameter (omp_atv_all = 7)
|
|
parameter (omp_atv_thread = 8)
|
|
parameter (omp_atv_pteam = 9)
|
|
parameter (omp_atv_cgroup = 10)
|
|
parameter (omp_atv_default_mem_fb = 11)
|
|
parameter (omp_atv_null_fb = 12)
|
|
parameter (omp_atv_abort_fb = 13)
|
|
parameter (omp_atv_allocator_fb = 14)
|
|
parameter (omp_atv_environment = 15)
|
|
parameter (omp_atv_nearest = 16)
|
|
parameter (omp_atv_blocked = 17)
|
|
parameter (omp_atv_interleaved = 18)
|
|
integer (omp_allocator_handle_kind) omp_null_allocator
|
|
integer (omp_allocator_handle_kind) omp_default_mem_alloc
|
|
integer (omp_allocator_handle_kind) omp_large_cap_mem_alloc
|
|
integer (omp_allocator_handle_kind) omp_const_mem_alloc
|
|
integer (omp_allocator_handle_kind) omp_high_bw_mem_alloc
|
|
integer (omp_allocator_handle_kind) omp_low_lat_mem_alloc
|
|
integer (omp_allocator_handle_kind) omp_cgroup_mem_alloc
|
|
integer (omp_allocator_handle_kind) omp_pteam_mem_alloc
|
|
integer (omp_allocator_handle_kind) omp_thread_mem_alloc
|
|
parameter (omp_null_allocator = 0)
|
|
parameter (omp_default_mem_alloc = 1)
|
|
parameter (omp_large_cap_mem_alloc = 2)
|
|
parameter (omp_const_mem_alloc = 3)
|
|
parameter (omp_high_bw_mem_alloc = 4)
|
|
parameter (omp_low_lat_mem_alloc = 5)
|
|
parameter (omp_cgroup_mem_alloc = 6)
|
|
parameter (omp_pteam_mem_alloc = 7)
|
|
parameter (omp_thread_mem_alloc = 8)
|
|
integer (omp_memspace_handle_kind) omp_default_mem_space
|
|
integer (omp_memspace_handle_kind) omp_large_cap_mem_space
|
|
integer (omp_memspace_handle_kind) omp_const_mem_space
|
|
integer (omp_memspace_handle_kind) omp_high_bw_mem_space
|
|
integer (omp_memspace_handle_kind) omp_low_lat_mem_space
|
|
parameter (omp_default_mem_space = 0)
|
|
parameter (omp_large_cap_mem_space = 1)
|
|
parameter (omp_const_mem_space = 2)
|
|
parameter (omp_high_bw_mem_space = 3)
|
|
parameter (omp_low_lat_mem_space = 4)
|
|
integer omp_initial_device, omp_invalid_device
|
|
parameter (omp_initial_device = -1)
|
|
parameter (omp_invalid_device = -4)
|
|
|
|
type omp_alloctrait
|
|
integer (omp_alloctrait_key_kind) key
|
|
integer (omp_alloctrait_val_kind) value
|
|
end type omp_alloctrait
|
|
|
|
external omp_init_lock, omp_init_nest_lock
|
|
external omp_init_lock_with_hint
|
|
external omp_init_nest_lock_with_hint
|
|
external omp_destroy_lock, omp_destroy_nest_lock
|
|
external omp_set_lock, omp_set_nest_lock
|
|
external omp_unset_lock, omp_unset_nest_lock
|
|
external omp_set_dynamic, omp_set_nested
|
|
external omp_set_num_threads
|
|
|
|
external omp_get_dynamic, omp_get_nested
|
|
logical(4) omp_get_dynamic, omp_get_nested
|
|
external omp_test_lock, omp_in_parallel
|
|
logical(4) omp_test_lock, omp_in_parallel
|
|
|
|
external omp_get_max_threads, omp_get_num_procs
|
|
integer(4) omp_get_max_threads, omp_get_num_procs
|
|
external omp_get_num_threads, omp_get_thread_num
|
|
integer(4) omp_get_num_threads, omp_get_thread_num
|
|
external omp_test_nest_lock
|
|
integer(4) omp_test_nest_lock
|
|
|
|
external omp_get_wtick, omp_get_wtime
|
|
double precision omp_get_wtick, omp_get_wtime
|
|
|
|
external omp_set_schedule, omp_get_schedule
|
|
external omp_get_thread_limit, omp_set_max_active_levels
|
|
external omp_get_max_active_levels, omp_get_level
|
|
external omp_get_ancestor_thread_num, omp_get_team_size
|
|
external omp_get_active_level
|
|
external omp_get_supported_active_levels
|
|
integer(4) omp_get_thread_limit, omp_get_max_active_levels
|
|
integer(4) omp_get_level, omp_get_ancestor_thread_num
|
|
integer(4) omp_get_team_size, omp_get_active_level
|
|
integer(4) omp_get_supported_active_levels
|
|
|
|
external omp_in_final
|
|
logical(4) omp_in_final
|
|
|
|
external omp_get_cancellation
|
|
logical(4) omp_get_cancellation
|
|
|
|
external omp_get_proc_bind
|
|
integer(omp_proc_bind_kind) omp_get_proc_bind
|
|
|
|
integer(4) omp_get_num_places
|
|
external omp_get_num_places
|
|
integer(4) omp_get_place_num_procs
|
|
external omp_get_place_num_procs
|
|
external omp_get_place_proc_ids
|
|
integer(4) omp_get_place_num
|
|
external omp_get_place_num
|
|
integer(4) omp_get_partition_num_places
|
|
external omp_get_partition_num_places
|
|
external omp_get_partition_place_nums
|
|
|
|
external omp_set_default_device, omp_get_default_device
|
|
external omp_get_num_devices, omp_get_num_teams
|
|
external omp_get_team_num
|
|
integer(4) omp_get_default_device, omp_get_num_devices
|
|
integer(4) omp_get_num_teams, omp_get_team_num
|
|
|
|
external omp_is_initial_device
|
|
logical(4) omp_is_initial_device
|
|
external omp_get_initial_device
|
|
integer(4) omp_get_initial_device
|
|
|
|
external omp_get_device_num
|
|
integer(4) omp_get_device_num
|
|
|
|
external omp_get_max_task_priority
|
|
integer(4) omp_get_max_task_priority
|
|
|
|
external omp_set_num_teams, omp_set_teams_thread_limit
|
|
external omp_get_max_teams, omp_get_teams_thread_limit
|
|
integer(4) omp_get_max_teams, omp_get_teams_thread_limit
|
|
|
|
external omp_fulfill_event
|
|
|
|
external omp_set_affinity_format, omp_get_affinity_format
|
|
external omp_display_affinity, omp_capture_affinity
|
|
integer(4) omp_get_affinity_format
|
|
integer(4) omp_capture_affinity
|
|
|
|
external omp_pause_resource, omp_pause_resource_all
|
|
integer(4) omp_pause_resource
|
|
integer(4) omp_pause_resource_all
|
|
|
|
external omp_init_allocator
|
|
integer (omp_allocator_handle_kind) omp_init_allocator
|
|
external omp_destroy_allocator
|
|
external omp_set_default_allocator
|
|
external omp_get_default_allocator
|
|
integer (omp_allocator_handle_kind) omp_get_default_allocator
|
|
|
|
external omp_display_env
|
|
|
|
interface
|
|
function omp_alloc (size, allocator) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_size_t
|
|
use, intrinsic :: omp_lib_kinds
|
|
type(c_ptr) :: omp_alloc
|
|
integer(c_size_t), value :: size
|
|
integer(omp_allocator_handle_kind), value :: allocator
|
|
end function omp_alloc
|
|
end interface
|
|
|
|
interface
|
|
function omp_aligned_alloc (alignment, size, allocator) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_size_t
|
|
use, intrinsic :: omp_lib_kinds
|
|
type(c_ptr) :: omp_aligned_alloc
|
|
integer(c_size_t), value :: alignment, size
|
|
integer(omp_allocator_handle_kind), value :: allocator
|
|
end function omp_aligned_alloc
|
|
end interface
|
|
|
|
interface
|
|
subroutine omp_free(ptr, allocator) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr
|
|
use, intrinsic :: omp_lib_kinds
|
|
type(c_ptr), value :: ptr
|
|
integer(omp_allocator_handle_kind), value :: allocator
|
|
end subroutine omp_free
|
|
end interface
|
|
|
|
interface
|
|
function omp_calloc (nmemb, size, allocator) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_size_t
|
|
use, intrinsic :: omp_lib_kinds
|
|
type(c_ptr) :: omp_calloc
|
|
integer(c_size_t), value :: nmemb, size
|
|
integer(omp_allocator_handle_kind), value :: allocator
|
|
end function omp_calloc
|
|
end interface
|
|
|
|
interface
|
|
function omp_aligned_calloc (alignment, nmemb, size, allocator) &
|
|
& bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_size_t
|
|
use, intrinsic :: omp_lib_kinds
|
|
type(c_ptr) :: omp_aligned_calloc
|
|
integer(c_size_t), value :: alignment, nmemb, size
|
|
integer(omp_allocator_handle_kind), value :: allocator
|
|
end function omp_aligned_calloc
|
|
end interface
|
|
|
|
interface
|
|
function omp_realloc (ptr, size, allocator, free_allocator) &
|
|
& bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_size_t
|
|
use, intrinsic :: omp_lib_kinds
|
|
type(c_ptr) :: omp_realloc
|
|
type(c_ptr), value :: ptr
|
|
integer(c_size_t), value :: size
|
|
integer(omp_allocator_handle_kind), value :: allocator
|
|
integer(omp_allocator_handle_kind), value :: free_allocator
|
|
end function omp_realloc
|
|
end interface
|
|
|
|
interface
|
|
function omp_target_alloc (size, device_num) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_size_t, c_int
|
|
type(c_ptr) :: omp_target_alloc
|
|
integer(c_size_t), value :: size
|
|
integer(c_int), value :: device_num
|
|
end function omp_target_alloc
|
|
end interface
|
|
|
|
interface
|
|
subroutine omp_target_free (device_ptr, device_num) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_int
|
|
type(c_ptr), value :: device_ptr
|
|
integer(c_int), value :: device_num
|
|
end subroutine omp_target_free
|
|
end interface
|
|
|
|
interface
|
|
function omp_target_is_present (ptr, device_num) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_int
|
|
integer(c_int) :: omp_target_is_present
|
|
type(c_ptr), value :: ptr
|
|
integer(c_int), value :: device_num
|
|
end function omp_target_is_present
|
|
end interface
|
|
|
|
interface
|
|
function omp_target_memcpy (dst, src, length, dst_offset, &
|
|
& src_offset, dst_device_num, &
|
|
& src_device_num) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_int, c_size_t
|
|
integer(c_int) :: omp_target_memcpy
|
|
type(c_ptr), value :: dst, src
|
|
integer(c_size_t), value :: length, dst_offset, src_offset
|
|
integer(c_int), value :: dst_device_num, src_device_num
|
|
end function omp_target_memcpy
|
|
end interface
|
|
|
|
interface
|
|
function omp_target_memcpy_async (dst, src, length, dst_offset, &
|
|
& src_offset, dst_device_num, &
|
|
& src_device_num, depobj_count, &
|
|
& depobj_list) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_int, c_size_t
|
|
import :: omp_depend_kind
|
|
integer(c_int) :: omp_target_memcpy_async
|
|
type(c_ptr), value :: dst, src
|
|
integer(c_size_t), value :: length, dst_offset, src_offset
|
|
integer(c_int), value :: dst_device_num, src_device_num
|
|
integer(c_int), value :: depobj_count
|
|
integer(omp_depend_kind), optional :: depobj_list(*)
|
|
end function omp_target_memcpy_async
|
|
end interface
|
|
|
|
interface
|
|
function omp_target_memcpy_rect (dst,src,element_size, num_dims, &
|
|
& volume, dst_offsets, &
|
|
& src_offsets, dst_dimensions, &
|
|
& src_dimensions, dst_device_num, &
|
|
& src_device_num) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_int, c_size_t
|
|
integer(c_int) :: omp_target_memcpy_rect
|
|
type(c_ptr), value :: dst, src
|
|
integer(c_size_t), value :: element_size
|
|
integer(c_int), value :: num_dims
|
|
integer(c_int), value :: dst_device_num, src_device_num
|
|
integer(c_size_t), intent(in) :: volume(*), dst_offsets(*)
|
|
integer(c_size_t), intent(in) :: src_offsets(*)
|
|
integer(c_size_t), intent(in) :: dst_dimensions(*)
|
|
integer(c_size_t), intent(in) :: src_dimensions(*)
|
|
end function omp_target_memcpy_rect
|
|
end interface
|
|
|
|
interface
|
|
function omp_target_memcpy_rect_async (dst,src,element_size, &
|
|
& num_dims, volume, &
|
|
& dst_offsets, src_offsets, &
|
|
& dst_dimensions, &
|
|
& src_dimensions, &
|
|
& dst_device_num, &
|
|
& src_device_num, &
|
|
& depobj_count, &
|
|
& depobj_list) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_int, c_size_t
|
|
import :: omp_depend_kind
|
|
integer(c_int) :: omp_target_memcpy_rect_async
|
|
type(c_ptr), value :: dst, src
|
|
integer(c_size_t), value :: element_size
|
|
integer(c_int), value :: num_dims, depobj_count
|
|
integer(c_int), value :: dst_device_num, src_device_num
|
|
integer(c_size_t), intent(in) :: volume(*), dst_offsets(*)
|
|
integer(c_size_t), intent(in) :: src_offsets(*)
|
|
integer(c_size_t), intent(in) :: dst_dimensions(*)
|
|
integer(c_size_t), intent(in) :: src_dimensions(*)
|
|
integer(omp_depend_kind), optional :: depobj_list(*)
|
|
end function omp_target_memcpy_rect_async
|
|
end interface
|
|
|
|
interface
|
|
function omp_target_associate_ptr (host_ptr, device_ptr, size, &
|
|
& device_offset, device_num) &
|
|
& bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_size_t, c_int
|
|
integer(c_int) :: omp_target_associate_ptr
|
|
type(c_ptr), value :: host_ptr, device_ptr
|
|
integer(c_size_t), value :: size, device_offset
|
|
integer(c_int), value :: device_num
|
|
end function omp_target_associate_ptr
|
|
end interface
|
|
|
|
interface
|
|
function omp_target_disassociate_ptr (ptr, device_num) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_int
|
|
integer(c_int) :: omp_target_disassociate_ptr
|
|
type(c_ptr), value :: ptr
|
|
integer(c_int), value :: device_num
|
|
end function omp_target_disassociate_ptr
|
|
end interface
|
|
|
|
interface
|
|
function omp_get_mapped_ptr (ptr, device_num) bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_int
|
|
type(c_ptr) :: omp_get_mapped_ptr
|
|
type(c_ptr), value :: ptr
|
|
integer(c_int), value :: device_num
|
|
end function omp_get_mapped_ptr
|
|
end interface
|
|
|
|
interface
|
|
function omp_target_is_accessible (ptr, size, device_num) &
|
|
& bind(c)
|
|
use, intrinsic :: iso_c_binding, only : c_ptr, c_size_t, c_int
|
|
integer(c_int) :: omp_target_is_accessible
|
|
type(c_ptr), value :: ptr
|
|
integer(c_size_t), value :: size
|
|
integer(c_int), value :: device_num
|
|
end function omp_target_is_accessible
|
|
end interface
|