| blob | ab668a5b70e41d2af14413326e54db9424f751a0 |
1 2014-12-17 Thomas Schwinge <thomas@codesourcery.com>
2 Julian Brown <julian@codesourcery.com>
3 David Malcolm <dmalcolm@redhat.com>
5 * configure.ac: Rename from GNU OpenMP Runtime Library to GNU
6 Offloading and Multi Processing Runtime Library. Change all
7 users.
9 2014-12-17 Thomas Schwinge <thomas@codesourcery.com>
10 Julian Brown <julian@codesourcery.com>
12 * plugin/Makefile.am: Rework into...
13 * plugin/Makefrag.am: ... this new file, and
14 * plugin/configure.ac: rework into...
15 * plugin/configfrag.ac: ... this new file. Change all users.
16 * configure.ac: Move plugin/offloading handling...
17 * plugin/configfrag.ac: ... here.
19 * env.c (initialize_env): Don't look for GCC_ACC_NOTIFY but for
20 GOMP_DEBUG. Document it in the libgomp manual.
21 * libgomp-plugin.h: Rename GOMP_PLUGIN_notify to
22 GOMP_PLUGIN_debug. Change all users.
23 * libgomp.h: Rename goacc_notify_var to gomp_debug_var,
24 gomp_vnotify to gomp_vdebug, and gomp_notify to gomp_debug.
25 Change all users. Add kind argument to gomp_vdebug and
26 gomp_debug. Change all users.
28 * libgomp_g.h: Remove names of formal parameters.
30 * libgomp_target.h: Rename ACC_dispatch_t to acc_dispatch_t.
31 Change all users.
32 * oacc-init.c: Rename _acc_init to acc_init_1, and _acc_shutdown
33 to acc_shutdown_1. Change all users.
34 * oacc-int.h: Rename ACC_register to goacc_register,
35 ACC_runtime_initialize to goacc_runtime_initialize,
36 ACC_save_and_set_bind to goacc_save_and_set_bind, ACC_restore_bind
37 to goacc_restore_bind, and ACC_lazy_initialize to
38 goacc_lazy_initialize. Change all users.
39 * plugin/plugin-nvptx.c: Rename cuErrorList to cuda_errlist,
40 cuErrorMsg to cuda_error, cuSymNames to cuda_symnames, PTX_inited
41 to ptx_inited, PTX_stream to ptx_stream, PTX_device to ptx_device,
42 PTX_event to ptx_event, PTX_event_type to ptx_event_type, PTX_init
43 to nvptx_init, , PTX_fini to nvptx_fini, PTX_open_device to
44 nvptx_open_device, PTX_close_device to nvptx_close_device,
45 PTX_get_num_devices to nvptx_get_num_devices, PTX_exec to
46 nvptx_exec, PTX_alloc to nvptx_alloc, PTX_free to nvptx_free,
47 PTX_host2dev to nvptx_host2dev, PTX_dev2host to nvptx_dev2host,
48 PTX_set_async to nvptx_set_async, PTX_async_test to
49 nvptx_async_test, PTX_async_test_all to nvptx_async_test_all,
50 PTX_wait to nvptx_wait, PTX_wait_async to nvptx_wait_async,
51 PTX_wait_all to nvptx_wait_all, PTX_wait_all_async to
52 nvptx_wait_all_async, PTX_get_current_cuda_device to
53 nvptx_get_current_cuda_device, PTX_get_current_cuda_context to
54 nvptx_get_current_cuda_context, PTX_get_cuda_stream to
55 nvptx_get_cuda_stream, PTX_set_cuda_stream to
56 nvptx_set_cuda_stream. Change all users.
58 * oacc-parallel.c (GOACC_kernels): Pass 0 instead of num_waits in
59 GOACC_parallel invocation.
61 * plugin/plugin-host.c: Remove all DEBUG code.
62 * plugin/plugin-nvptx.c: Likewise.
64 * plugin/plugin-host.c (GOMP_OFFLOAD_get_caps): Don't claim
65 TARGET_CAP_OPENMP_400.
67 * testsuite/libgomp.oacc-c-c++-common/lib-11.c: Restrict to target
68 openacc_nvidia_accel_selected.
70 * testsuite/libgomp.oacc-c-c++-common/lib-38.c: Remove wrong
71 check.
73 * testsuite/libgomp.oacc-c-c++-common/lib-9.c: Fix wrong check.
75 2014-11-14 Tom de Vries <tom@codesourcery.com>
77 * Makefile.am: Add missing dependency "openacc.mod: openacc.lo".
78 * Makefile.in: Regenerate.
80 2014-11-14 Tom de Vries <tom@codesourcery.com>
82 * configure.tgt: Handle case that $enable_linux_futex is empty.
84 2014-11-14 Thomas Schwinge <thomas@codesourcery.com>
86 * libgomp.texi (Reporting Bugs): Mention the "openacc" Bugzilla
87 keyword.
89 2014-11-13 Thomas Schwinge <thomas@codesourcery.com>
91 * testsuite/libgomp.oacc-c-c++-common/context-2.c: Fix data
92 clause.
94 * target.c (gomp_map_vars_existing): Error out if "force"
95 semantics.
96 (gomp_map_vars): Actually pass kinds to gomp_map_vars_existing.
97 Remove FIXMEs.
98 * testsuite/libgomp.oacc-c-c++-common/data-already-1.c: New file.
99 * testsuite/libgomp.oacc-c-c++-common/data-already-2.c: Likewise.
100 * testsuite/libgomp.oacc-c-c++-common/data-already-3.c: Likewise.
101 * testsuite/libgomp.oacc-c-c++-common/data-already-4.c: Likewise.
102 * testsuite/libgomp.oacc-c-c++-common/data-already-5.c: Likewise.
103 * testsuite/libgomp.oacc-c-c++-common/data-already-6.c: Likewise.
104 * testsuite/libgomp.oacc-c-c++-common/data-already-7.c: Likewise.
105 * testsuite/libgomp.oacc-c-c++-common/data-already-8.c: Likewise.
106 * testsuite/libgomp.oacc-fortran/data-already-1.f: Likewise.
107 * testsuite/libgomp.oacc-fortran/data-already-2.f: Likewise.
108 * testsuite/libgomp.oacc-fortran/data-already-3.f: Likewise.
109 * testsuite/libgomp.oacc-fortran/data-already-4.f: Likewise.
110 * testsuite/libgomp.oacc-fortran/data-already-5.f: Likewise.
111 * testsuite/libgomp.oacc-fortran/data-already-6.f: Likewise.
112 * testsuite/libgomp.oacc-fortran/data-already-7.f: Likewise.
113 * testsuite/libgomp.oacc-fortran/data-already-8.f: Likewise.
115 2014-11-12 Thomas Schwinge <thomas@codesourcery.com>
117 * testsuite/libgomp.oacc-c-c++-common/collapse-4.c: New file.
118 * testsuite/libgomp.oacc-c/collapse-4.c: Turn into an execution
119 test, check result.
120 * testsuite/libgomp.oacc-c-c++-common/data-2.c: Update.
121 * testsuite/libgomp.oacc-c-c++-common/data-3.c: Likewise.
123 2014-11-11 Thomas Schwinge <thomas@codesourcery.com>
125 * plugin-nvptx.c: Remove.
127 2014-11-07 Tom de Vries <tom@codesourcery.com>
129 * testsuite/libgomp.oacc-c-c++-common/lib-66.c: Skip for shared memory
130 accelerators.
131 (main): Use acc_device_default instead of acc_device_nvidia.
133 2014-11-06 Julian Brown <julian@codesourcery.com>
135 * oacc-init.c (resolve_device, _acc_init): Fix init_device_func
136 hook naming.
137 * plugin/plugin-host.c (GOMP_OFFLOAD_openacc_avail): Remove.
138 (host_dispatch): Don't set avail_func hook.
139 * plugin/configure.ac (libgomp-test-support.exp): Add to
140 AC_CONFIG_FILES.
141 * plugin/configure: Regenerate.
142 * testsuite/libgomp-test-support.exp.in: Move from here...
143 * plugin/libgomp-test-support.exp.in: ...to here.
144 * plugin/Makefile.in: Regenerate.
145 * testsuite/lib/libgomp.exp (libgomp-test-support.exp): Find in
146 plugin dir, for now.
147 * testsuite/Makefile.in: Regenerate.
148 * configure.ac (testsuite/libgomp-test-support.exp): Remove from
149 AC_CONFIG_FILES.
150 * config.h.in: Regenerate.
151 * configure: Regenerate.
153 2014-11-05 Julian Brown <julian@codesourcery.com>
155 * Makefile.am (SUBDIRS): Add plugin.
156 (DIST_SUBDIRS): Define.
157 (libgomp_plugin_nvptx_*): Remove nvptx support from here.
158 (libgomp_plugin_host_nonshm_*): Likewise.
159 * Makefile.in: Regenerate.
160 * configure: Regenerate.
161 * oacc-host.c: Replace with #include of plugin/plugin-host.c code,
162 move implementation to the latter.
163 * plugin/plugin-host.c: New file.
164 * plugin-nvptx.c: Copy to...
165 * plugin/plugin-nvptx.c: New file.
166 * plugin/Makefile.am: New.
167 * plugin/Makefile.in: Regenerate.
168 * plugin/aclocal.m4: Regenerate.
169 * plugin/configure: Regenerate.
171 2014-11-05 Julian Brown <julian@codesourcery.com>
173 * oacc-host.c: Add GOMP_OFFLOAD_ prefix for plugin hooks. Rename
174 device_init to init_device, device_fini to fini_device,
175 offload_register to register_image and remove extraneous "device_"
176 from device_alloc, device_free, device_dev2host, device_host2dev and
177 device_run.
178 (host_dispatch): Use new names for hooks.
179 * oacc-init.c: Use new names for hooks, throughout.
180 * plugin-nvptx.c: Likewise.
181 * target.c: Likewise.
182 (gomp_load_plugin_for_device): Likewise. Look for new hook names.
183 * target.h (gomp_device_descr): Use new hook names.
185 2014-11-05 Thomas Schwinge <thomas@codesourcery.com>
187 * testsuite/libgomp.oacc-c-c++-common/update-1-2.c: New file.
188 * testsuite/libgomp.oacc-fortran/data-4-2.f90: Likewise.
189 * testsuite/libgomp.oacc-fortran/data-4.f90: In one instance, use
190 the self clause instead of host clause.
192 * testsuite/libgomp.oacc-c/cache-1.c: Remove directives that are
193 expected to fail, and rename the file to...
194 * testsuite/libgomp.oacc-c-c++-common/cache-1.c: ... this.
195 * testsuite/libgomp.oacc-c++/cache-1.C: Remove file.
197 2014-11-05 James Norris <jnorris@codesourcery.com>
199 * testsuite/libgomp.oacc-c/cache-1.c: New file.
200 * testsuite/libgomp.oacc-c++/cache-1.C: Likewise.
202 2014-11-05 Thomas Schwinge <thomas@codesourcery.com>
203 James Norris <jnorris@codesourcery.com>
205 * testsuite/libgomp.oacc-c++/c++.exp: Enable
206 libgomp.oacc-c-c++-common testing.
207 * testsuite/libgomp.oacc-c/c.exp: Likewise.
208 * testsuite/libgomp.oacc-c/abort-2.c: Rename to...
209 * testsuite/libgomp.oacc-c-c++-common/abort-2.c: ... this.
210 * testsuite/libgomp.oacc-c/abort.c: Rename to...
211 * testsuite/libgomp.oacc-c-c++-common/abort.c: ... this.
212 * testsuite/libgomp.oacc-c/acc_on_device-1.c: Rename to...
213 * testsuite/libgomp.oacc-c-c++-common/acc_on_device-1.c: ... this.
214 * testsuite/libgomp.oacc-c/clauses-1.c: Rename to...
215 * testsuite/libgomp.oacc-c-c++-common/clauses-1.c: ... this.
216 * testsuite/libgomp.oacc-c/clauses-2.c: Rename to...
217 * testsuite/libgomp.oacc-c-c++-common/clauses-2.c: ... this.
218 * testsuite/libgomp.oacc-c/context-1.c: Rename to...
219 * testsuite/libgomp.oacc-c-c++-common/context-1.c: ... this.
220 * testsuite/libgomp.oacc-c/context-2.c: Rename to...
221 * testsuite/libgomp.oacc-c-c++-common/context-2.c: ... this.
222 * testsuite/libgomp.oacc-c/context-3.c: Rename to...
223 * testsuite/libgomp.oacc-c-c++-common/context-3.c: ... this.
224 * testsuite/libgomp.oacc-c/context-4.c: Rename to...
225 * testsuite/libgomp.oacc-c-c++-common/context-4.c: ... this.
226 * testsuite/libgomp.oacc-c/data-1.c: Rename to...
227 * testsuite/libgomp.oacc-c-c++-common/data-1.c: ... this.
228 * testsuite/libgomp.oacc-c/data-2.c: Rename to...
229 * testsuite/libgomp.oacc-c-c++-common/data-2.c: ... this.
230 * testsuite/libgomp.oacc-c/data-3.c: Rename to...
231 * testsuite/libgomp.oacc-c-c++-common/data-3.c: ... this.
232 * testsuite/libgomp.oacc-c/deviceptr-1.c: Rename to...
233 * testsuite/libgomp.oacc-c-c++-common/deviceptr-1.c: ... this.
234 * testsuite/libgomp.oacc-c/if-1.c: Rename to...
235 * testsuite/libgomp.oacc-c-c++-common/if-1.c: ... this.
236 * testsuite/libgomp.oacc-c/kernels-1.c: Rename to...
237 * testsuite/libgomp.oacc-c-c++-common/kernels-1.c: ... this.
238 * testsuite/libgomp.oacc-c/lib-1.c: Rename to...
239 * testsuite/libgomp.oacc-c-c++-common/lib-1.c: ... this.
240 * testsuite/libgomp.oacc-c/lib-10.c: Rename to...
241 * testsuite/libgomp.oacc-c-c++-common/lib-10.c: ... this.
242 * testsuite/libgomp.oacc-c/lib-11.c: Rename to...
243 * testsuite/libgomp.oacc-c-c++-common/lib-11.c: ... this.
244 * testsuite/libgomp.oacc-c/lib-12.c: Rename to...
245 * testsuite/libgomp.oacc-c-c++-common/lib-12.c: ... this.
246 * testsuite/libgomp.oacc-c/lib-13.c: Rename to...
247 * testsuite/libgomp.oacc-c-c++-common/lib-13.c: ... this.
248 * testsuite/libgomp.oacc-c/lib-14.c: Rename to...
249 * testsuite/libgomp.oacc-c-c++-common/lib-14.c: ... this.
250 * testsuite/libgomp.oacc-c/lib-15.c: Rename to...
251 * testsuite/libgomp.oacc-c-c++-common/lib-15.c: ... this.
252 * testsuite/libgomp.oacc-c/lib-16.c: Rename to...
253 * testsuite/libgomp.oacc-c-c++-common/lib-16.c: ... this.
254 * testsuite/libgomp.oacc-c/lib-17.c: Rename to...
255 * testsuite/libgomp.oacc-c-c++-common/lib-17.c: ... this.
256 * testsuite/libgomp.oacc-c/lib-18.c: Rename to...
257 * testsuite/libgomp.oacc-c-c++-common/lib-18.c: ... this.
258 * testsuite/libgomp.oacc-c/lib-19.c: Rename to...
259 * testsuite/libgomp.oacc-c-c++-common/lib-19.c: ... this.
260 * testsuite/libgomp.oacc-c/lib-2.c: Rename to...
261 * testsuite/libgomp.oacc-c-c++-common/lib-2.c: ... this.
262 * testsuite/libgomp.oacc-c/lib-20.c: Rename to...
263 * testsuite/libgomp.oacc-c-c++-common/lib-20.c: ... this.
264 * testsuite/libgomp.oacc-c/lib-21.c: Rename to...
265 * testsuite/libgomp.oacc-c-c++-common/lib-21.c: ... this.
266 * testsuite/libgomp.oacc-c/lib-22.c: Rename to...
267 * testsuite/libgomp.oacc-c-c++-common/lib-22.c: ... this.
268 * testsuite/libgomp.oacc-c/lib-23.c: Rename to...
269 * testsuite/libgomp.oacc-c-c++-common/lib-23.c: ... this.
270 * testsuite/libgomp.oacc-c/lib-24.c: Rename to...
271 * testsuite/libgomp.oacc-c-c++-common/lib-24.c: ... this.
272 * testsuite/libgomp.oacc-c/lib-25.c: Rename to...
273 * testsuite/libgomp.oacc-c-c++-common/lib-25.c: ... this.
274 * testsuite/libgomp.oacc-c/lib-26.c: Rename to...
275 * testsuite/libgomp.oacc-c-c++-common/lib-26.c: ... this.
276 * testsuite/libgomp.oacc-c/lib-27.c: Rename to...
277 * testsuite/libgomp.oacc-c-c++-common/lib-27.c: ... this.
278 * testsuite/libgomp.oacc-c/lib-28.c: Rename to...
279 * testsuite/libgomp.oacc-c-c++-common/lib-28.c: ... this.
280 * testsuite/libgomp.oacc-c/lib-29.c: Rename to...
281 * testsuite/libgomp.oacc-c-c++-common/lib-29.c: ... this.
282 * testsuite/libgomp.oacc-c/lib-3.c: Rename to...
283 * testsuite/libgomp.oacc-c-c++-common/lib-3.c: ... this.
284 * testsuite/libgomp.oacc-c/lib-30.c: Rename to...
285 * testsuite/libgomp.oacc-c-c++-common/lib-30.c: ... this.
286 * testsuite/libgomp.oacc-c/lib-31.c: Rename to...
287 * testsuite/libgomp.oacc-c-c++-common/lib-31.c: ... this.
288 * testsuite/libgomp.oacc-c/lib-32.c: Rename to...
289 * testsuite/libgomp.oacc-c-c++-common/lib-32.c: ... this.
290 * testsuite/libgomp.oacc-c/lib-33.c: Rename to...
291 * testsuite/libgomp.oacc-c-c++-common/lib-33.c: ... this.
292 * testsuite/libgomp.oacc-c/lib-34.c: Rename to...
293 * testsuite/libgomp.oacc-c-c++-common/lib-34.c: ... this.
294 * testsuite/libgomp.oacc-c/lib-35.c: Rename to...
295 * testsuite/libgomp.oacc-c-c++-common/lib-35.c: ... this.
296 * testsuite/libgomp.oacc-c/lib-36.c: Rename to...
297 * testsuite/libgomp.oacc-c-c++-common/lib-36.c: ... this.
298 * testsuite/libgomp.oacc-c/lib-37.c: Rename to...
299 * testsuite/libgomp.oacc-c-c++-common/lib-37.c: ... this.
300 * testsuite/libgomp.oacc-c/lib-38.c: Rename to...
301 * testsuite/libgomp.oacc-c-c++-common/lib-38.c: ... this.
302 * testsuite/libgomp.oacc-c/lib-39.c: Rename to...
303 * testsuite/libgomp.oacc-c-c++-common/lib-39.c: ... this.
304 * testsuite/libgomp.oacc-c/lib-4.c: Rename to...
305 * testsuite/libgomp.oacc-c-c++-common/lib-4.c: ... this.
306 * testsuite/libgomp.oacc-c/lib-40.c: Rename to...
307 * testsuite/libgomp.oacc-c-c++-common/lib-40.c: ... this.
308 * testsuite/libgomp.oacc-c/lib-41.c: Rename to...
309 * testsuite/libgomp.oacc-c-c++-common/lib-41.c: ... this.
310 * testsuite/libgomp.oacc-c/lib-42.c: Rename to...
311 * testsuite/libgomp.oacc-c-c++-common/lib-42.c: ... this.
312 * testsuite/libgomp.oacc-c/lib-43.c: Rename to...
313 * testsuite/libgomp.oacc-c-c++-common/lib-43.c: ... this.
314 * testsuite/libgomp.oacc-c/lib-44.c: Rename to...
315 * testsuite/libgomp.oacc-c-c++-common/lib-44.c: ... this.
316 * testsuite/libgomp.oacc-c/lib-45.c: Rename to...
317 * testsuite/libgomp.oacc-c-c++-common/lib-45.c: ... this.
318 * testsuite/libgomp.oacc-c/lib-46.c: Rename to...
319 * testsuite/libgomp.oacc-c-c++-common/lib-46.c: ... this.
320 * testsuite/libgomp.oacc-c/lib-47.c: Rename to...
321 * testsuite/libgomp.oacc-c-c++-common/lib-47.c: ... this.
322 * testsuite/libgomp.oacc-c/lib-48.c: Rename to...
323 * testsuite/libgomp.oacc-c-c++-common/lib-48.c: ... this.
324 * testsuite/libgomp.oacc-c/lib-49.c: Rename to...
325 * testsuite/libgomp.oacc-c-c++-common/lib-49.c: ... this.
326 * testsuite/libgomp.oacc-c/lib-5.c: Rename to...
327 * testsuite/libgomp.oacc-c-c++-common/lib-5.c: ... this.
328 * testsuite/libgomp.oacc-c/lib-50.c: Rename to...
329 * testsuite/libgomp.oacc-c-c++-common/lib-50.c: ... this.
330 * testsuite/libgomp.oacc-c/lib-51.c: Rename to...
331 * testsuite/libgomp.oacc-c-c++-common/lib-51.c: ... this.
332 * testsuite/libgomp.oacc-c/lib-52.c: Rename to...
333 * testsuite/libgomp.oacc-c-c++-common/lib-52.c: ... this.
334 * testsuite/libgomp.oacc-c/lib-53.c: Rename to...
335 * testsuite/libgomp.oacc-c-c++-common/lib-53.c: ... this.
336 * testsuite/libgomp.oacc-c/lib-54.c: Rename to...
337 * testsuite/libgomp.oacc-c-c++-common/lib-54.c: ... this.
338 * testsuite/libgomp.oacc-c/lib-55.c: Rename to...
339 * testsuite/libgomp.oacc-c-c++-common/lib-55.c: ... this.
340 * testsuite/libgomp.oacc-c/lib-56.c: Rename to...
341 * testsuite/libgomp.oacc-c-c++-common/lib-56.c: ... this.
342 * testsuite/libgomp.oacc-c/lib-57.c: Rename to...
343 * testsuite/libgomp.oacc-c-c++-common/lib-57.c: ... this.
344 * testsuite/libgomp.oacc-c/lib-58.c: Rename to...
345 * testsuite/libgomp.oacc-c-c++-common/lib-58.c: ... this.
346 * testsuite/libgomp.oacc-c/lib-59.c: Rename to...
347 * testsuite/libgomp.oacc-c-c++-common/lib-59.c: ... this.
348 * testsuite/libgomp.oacc-c/lib-6.c: Rename to...
349 * testsuite/libgomp.oacc-c-c++-common/lib-6.c: ... this.
350 * testsuite/libgomp.oacc-c/lib-60.c: Rename to...
351 * testsuite/libgomp.oacc-c-c++-common/lib-60.c: ... this.
352 * testsuite/libgomp.oacc-c/lib-61.c: Rename to...
353 * testsuite/libgomp.oacc-c-c++-common/lib-61.c: ... this.
354 * testsuite/libgomp.oacc-c/lib-62.c: Rename to...
355 * testsuite/libgomp.oacc-c-c++-common/lib-62.c: ... this.
356 * testsuite/libgomp.oacc-c/lib-63.c: Rename to...
357 * testsuite/libgomp.oacc-c-c++-common/lib-63.c: ... this.
358 * testsuite/libgomp.oacc-c/lib-64.c: Rename to...
359 * testsuite/libgomp.oacc-c-c++-common/lib-64.c: ... this.
360 * testsuite/libgomp.oacc-c/lib-65.c: Rename to...
361 * testsuite/libgomp.oacc-c-c++-common/lib-65.c: ... this.
362 * testsuite/libgomp.oacc-c/lib-66.c: Rename to...
363 * testsuite/libgomp.oacc-c-c++-common/lib-66.c: ... this.
364 * testsuite/libgomp.oacc-c/lib-67.c: Rename to...
365 * testsuite/libgomp.oacc-c-c++-common/lib-67.c: ... this.
366 * testsuite/libgomp.oacc-c/lib-68.c: Rename to...
367 * testsuite/libgomp.oacc-c-c++-common/lib-68.c: ... this.
368 * testsuite/libgomp.oacc-c/lib-69.c: Rename to...
369 * testsuite/libgomp.oacc-c-c++-common/lib-69.c: ... this.
370 * testsuite/libgomp.oacc-c/lib-7.c: Rename to...
371 * testsuite/libgomp.oacc-c-c++-common/lib-7.c: ... this.
372 * testsuite/libgomp.oacc-c/lib-70.c: Rename to...
373 * testsuite/libgomp.oacc-c-c++-common/lib-70.c: ... this.
374 * testsuite/libgomp.oacc-c/lib-71.c: Rename to...
375 * testsuite/libgomp.oacc-c-c++-common/lib-71.c: ... this.
376 * testsuite/libgomp.oacc-c/lib-72.c: Rename to...
377 * testsuite/libgomp.oacc-c-c++-common/lib-72.c: ... this.
378 * testsuite/libgomp.oacc-c/lib-73.c: Rename to...
379 * testsuite/libgomp.oacc-c-c++-common/lib-73.c: ... this.
380 * testsuite/libgomp.oacc-c/lib-74.c: Rename to...
381 * testsuite/libgomp.oacc-c-c++-common/lib-74.c: ... this.
382 * testsuite/libgomp.oacc-c/lib-75.c: Rename to...
383 * testsuite/libgomp.oacc-c-c++-common/lib-75.c: ... this.
384 * testsuite/libgomp.oacc-c/lib-76.c: Rename to...
385 * testsuite/libgomp.oacc-c-c++-common/lib-76.c: ... this.
386 * testsuite/libgomp.oacc-c/lib-77.c: Rename to...
387 * testsuite/libgomp.oacc-c-c++-common/lib-77.c: ... this.
388 * testsuite/libgomp.oacc-c/lib-78.c: Rename to...
389 * testsuite/libgomp.oacc-c-c++-common/lib-78.c: ... this.
390 * testsuite/libgomp.oacc-c/lib-79.c: Rename to...
391 * testsuite/libgomp.oacc-c-c++-common/lib-79.c: ... this.
392 * testsuite/libgomp.oacc-c/lib-80.c: Rename to...
393 * testsuite/libgomp.oacc-c-c++-common/lib-80.c: ... this.
394 * testsuite/libgomp.oacc-c/lib-81.c: Rename to...
395 * testsuite/libgomp.oacc-c-c++-common/lib-81.c: ... this.
396 * testsuite/libgomp.oacc-c/lib-82.c: Rename to...
397 * testsuite/libgomp.oacc-c-c++-common/lib-82.c: ... this.
398 * testsuite/libgomp.oacc-c/lib-83.c: Rename to...
399 * testsuite/libgomp.oacc-c-c++-common/lib-83.c: ... this.
400 * testsuite/libgomp.oacc-c/lib-84.c: Rename to...
401 * testsuite/libgomp.oacc-c-c++-common/lib-84.c: ... this.
402 * testsuite/libgomp.oacc-c/lib-85.c: Rename to...
403 * testsuite/libgomp.oacc-c-c++-common/lib-85.c: ... this.
404 * testsuite/libgomp.oacc-c/lib-86.c: Rename to...
405 * testsuite/libgomp.oacc-c-c++-common/lib-86.c: ... this.
406 * testsuite/libgomp.oacc-c/lib-87.c: Rename to...
407 * testsuite/libgomp.oacc-c-c++-common/lib-87.c: ... this.
408 * testsuite/libgomp.oacc-c/lib-88.c: Rename to...
409 * testsuite/libgomp.oacc-c-c++-common/lib-88.c: ... this.
410 * testsuite/libgomp.oacc-c/lib-89.c: Rename to...
411 * testsuite/libgomp.oacc-c-c++-common/lib-89.c: ... this.
412 * testsuite/libgomp.oacc-c/lib-9.c: Rename to...
413 * testsuite/libgomp.oacc-c-c++-common/lib-9.c: ... this.
414 * testsuite/libgomp.oacc-c/lib-90.c: Rename to...
415 * testsuite/libgomp.oacc-c-c++-common/lib-90.c: ... this.
416 * testsuite/libgomp.oacc-c/lib-91.c: Rename to...
417 * testsuite/libgomp.oacc-c-c++-common/lib-91.c: ... this.
418 * testsuite/libgomp.oacc-c/lib-92.c: Rename to...
419 * testsuite/libgomp.oacc-c-c++-common/lib-92.c: ... this.
420 * testsuite/libgomp.oacc-c/nested-1.c: Rename to...
421 * testsuite/libgomp.oacc-c-c++-common/nested-1.c: ... this.
422 * testsuite/libgomp.oacc-c/nested-2.c: Rename to...
423 * testsuite/libgomp.oacc-c-c++-common/nested-2.c: ... this.
424 * testsuite/libgomp.oacc-c/offset-1.c: Rename to...
425 * testsuite/libgomp.oacc-c-c++-common/offset-1.c: ... this.
426 * testsuite/libgomp.oacc-c/parallel-1.c: Rename to...
427 * testsuite/libgomp.oacc-c-c++-common/parallel-1.c: ... this.
428 * testsuite/libgomp.oacc-c/pointer-align-1.c: Rename to...
429 * testsuite/libgomp.oacc-c-c++-common/pointer-align-1.c: ... this.
430 * testsuite/libgomp.oacc-c/present-1.c: Rename to...
431 * testsuite/libgomp.oacc-c-c++-common/present-1.c: ... this.
432 * testsuite/libgomp.oacc-c/present-2.c: Rename to...
433 * testsuite/libgomp.oacc-c-c++-common/present-2.c: ... this.
434 * testsuite/libgomp.oacc-c/reduction-1.c: Rename to...
435 * testsuite/libgomp.oacc-c-c++-common/reduction-1.c: ... this.
436 * testsuite/libgomp.oacc-c/reduction-2.c: Rename to...
437 * testsuite/libgomp.oacc-c-c++-common/reduction-2.c: ... this.
438 * testsuite/libgomp.oacc-c/reduction-3.c: Rename to...
439 * testsuite/libgomp.oacc-c-c++-common/reduction-3.c: ... this.
440 * testsuite/libgomp.oacc-c/reduction-4.c: Rename to...
441 * testsuite/libgomp.oacc-c-c++-common/reduction-4.c: ... this.
442 * testsuite/libgomp.oacc-c/reduction-5.c: Rename to...
443 * testsuite/libgomp.oacc-c-c++-common/reduction-5.c: ... this.
444 * testsuite/libgomp.oacc-c/reduction-initial-1.c: Rename to...
445 * testsuite/libgomp.oacc-c-c++-common/reduction-initial-1.c: ... this.
446 * testsuite/libgomp.oacc-c/subr.cu: Rename to...
447 * testsuite/libgomp.oacc-c-c++-common/subr.cu: ... this.
448 * testsuite/libgomp.oacc-c/subr.ptx: Rename to...
449 * testsuite/libgomp.oacc-c-c++-common/subr.ptx: ... this.
450 * testsuite/libgomp.oacc-c/timer.h: Rename to...
451 * testsuite/libgomp.oacc-c-c++-common/timer.h: ... this.
452 * testsuite/libgomp.oacc-c/update-1.c: Rename to...
453 * testsuite/libgomp.oacc-c-c++-common/update-1.c: ... this.
455 2014-11-05 Thomas Schwinge <thomas@codesourcery.com>
457 * libgomp.texi: Update for OpenACC.
459 * target.h (struct ACC_dispatch_t): Remove avail_func. Update all
460 users.
461 * oacc-host.c (openacc_avail): Likewise.
462 * plugin-nvptx.c (PTX_avail, openacc_avail): Likewise.
463 * libgomp.texi (acc_get_num_devices): Revise.
465 * testsuite/libgomp.oacc-c/goacc_kernels.c: Remove file.
466 * testsuite/libgomp.oacc-c/goacc_parallel.c: Remove file.
468 2014-11-04 Cesar Philippidis <cesar@codesourcery.com>
470 * testsuite/libgomp.oacc-fortran/routine-1.f90: New test.
471 * testsuite/libgomp.oacc-fortran/routine-2.f90: New test.
472 * testsuite/libgomp.oacc-fortran/routine-3.f90: New test.
473 * testsuite/libgomp.oacc-fortran/routine-4.f90: New test.
475 2014-11-04 Thomas Schwinge <thomas@codesourcery.com>
477 * testsuite/libgomp.oacc-c/reduction-initial-1.c
478 [ACC_DEVICE_TYPE_host_nonshm]: Remove special-casing for N.
480 2014-11-03 Cesar Philippidis <cesar@codesourcery.com>
481 Thomas Schwinge <thomas@codesourcery.com>
483 * libgomp.map (GOACC_get_thread_num): Declare.
484 (GOACC_get_num_threads): Declare.
485 * libgomp_g.h (GOACC_get_thread_num): Declare.
486 (GOACC_get_num_threads): Declare.
487 * oacc-parallel.c (GOACC_parallel): Handle num_gangs.
488 (GOACC_get_num_threads): New function.
489 (GOACC_get_thread_num): New function.
490 * oacc-ptx.h: New file.
491 * plugin-nvptx.c (ABORT_PTX): Remove macro. Move to oacc-ptx.h.
492 (ACC_ON_DEVICE_PTX): Likewise.
493 (link_ptx): Also link ptx code defined by GOACC_INTERNAL_PTX.
494 (PTX_exec): Handle gangs/CTAs.
495 * testsuite/libgomp.oacc-c/reduction-1.c: New test.
496 * testsuite/libgomp.oacc-c/reduction-2.c: New test.
497 * testsuite/libgomp.oacc-c/reduction-3.c: New test.
498 * testsuite/libgomp.oacc-c/reduction-4.c: New test.
499 * testsuite/libgomp.oacc-c/reduction-5.: New test.
500 * testsuite/libgomp.oacc-c/reduction-initial-1.c: New test.
501 * testsuite/libgomp.oacc-fortran/reduction-1.f90: New test.
502 * testsuite/libgomp.oacc-fortran/reduction-2.f90: New test.
503 * testsuite/libgomp.oacc-fortran/reduction-3.f90: New test.
504 * testsuite/libgomp.oacc-fortran/reduction-4.f90: New test.
505 * testsuite/libgomp.oacc-fortran/reduction-5.f90: New test.
506 * testsuite/libgomp.oacc-fortran/reduction-6.f90: New test.
508 2014-11-03 Cesar Philippidis <cesar@codesourcery.com>
510 * libgomp.map (GOACC_enter_exit_data): Declare as global.
511 * libgomp_g.h (GOACC_enter_exit_data): Declare.
512 (GOACC_update): Declare.
513 (gomp_acc_insert_pointer): Declare.
514 (gomp_acc_remove_pointer): Declare.
515 * oacc-mem.c (gomp_acc_insert_pointer): New function.
516 (gomp_acc_remove_pointer): New function.
517 * oacc-parallel.c (find_pset): New function.
518 (GOACC_enter_exit_data): New function.
519 (GOACC_update): Handle GOMP_MAP_TO_PSET.
520 * testsuite/libgomp.oacc-c/data-2.c: New test.
521 * testsuite/libgomp.oacc-c/data-3.c: New test.
522 * testsuite/libgomp.oacc-fortran/data-1.f90: New test.
523 * testsuite/libgomp.oacc-fortran/data-2.f90: New test.
524 * testsuite/libgomp.oacc-fortran/data-3.f90: New test.
525 * testsuite/libgomp.oacc-fortran/data-4.f90: New test.
527 2014-10-31 Cesar Philippidis <cesar@codesourcery.com>
529 * testsuite/libgomp.oacc-fortran/asyncwait-1.f90: New test.
530 * testsuite/libgomp.oacc-fortran/asyncwait-2.f90: New test.
531 * testsuite/libgomp.oacc-fortran/asyncwait-3.f90: New test.
533 2014-10-31 Thomas Schwinge <thomas@codesourcery.com>
535 * configure.ac (CUDA_DRIVER_INCLUDE, CUDA_DRIVER_LIB): New
536 substituted variables.
537 (testsuite/libgomp-test-support.exp): Instantiate file.
538 * Makefile.in: Regenerate.
539 * configure: Likewise.
540 * testsuite/Makefile.in: Likewise.
541 * testsuite/libgomp-test-support.exp.in: New file.
542 * testsuite/lib/libgomp.exp: Load it.
543 (libgomp_init): For build-tree testing, add the CUDA paths to
544 ALWAYS_CFLAGS and always_ld_library_path.
546 2014-10-30 Julian Brown <julian@codesourcery.com>
548 * target.c (gomp_map_vars): Remove MM argument.
549 (GOMP_target, GOMP_target_data): Update calls to gomp_map_vars.
550 * oacc-mem.c (acc_map_data, present_create_copy): Update calls to
551 gomp_map_vars.
552 * oacc-parallel.c (GOACC_parallel, GOACC_data_start): Likewise.
553 * target.h (gomp_map_vars): Update prototype.
555 2014-10-30 Julian Brown <julian@codesourcery.com>
557 * oacc-host.c (DEBUG): Remove undefine.
558 * plugin-nvptx.c (DEBUG, DISABLE_ASYNC): Remove comment-out macro
559 definitions.
560 * target.c (dump_mappings): Remove debugging function.
562 2014-10-30 Julian Brown <julian@codesourcery.com>
564 * target.c (gomp_load_plugin_for_device): Only call get_caps once.
565 (gomp_find_available_plugins): ...and don't call it again here.
567 2014-10-30 Julian Brown <julian@codesourcery.com>
569 * env.c (goacc_notify_var): New.
570 (initialize_env): Use above instead of
571 gomp_global_icv.acc_notify_var.
572 * error.c (gomp_vnotify): Use goacc_notify_var.
573 (gomp_notify): Fix formatting.
574 * libgomp.h (gomp_task_icv): Remove acc_notify_var field.
575 (goacc_notify_var): Add extern declaration.
577 2014-10-30 Julian Brown <julian@codesourcery.com>
579 * env.c (goacc_parse_device_num): Remove.
580 (initialize_env): Use parse_int instead of goacc_parse_device_num.
581 * oacc-init.c (lazy_open): Add bounds check for device number.
583 2014-10-30 Julian Brown <julian@codesourcery.com>
585 * env.c (oacc-int.h): Include.
586 * libgomp-plugin.h (GOMP_PLUGIN_async_unmap_vars): Don't declare
587 here.
588 * libgomp.map (PLUGIN_1.0): Add GOMP_PLUGIN_acc_thread symbol.
589 * oacc-async.c (oacc-int.h): Include.
590 (acc_async_test, acc_async_test_all, acc_wait, acc_wait_async)
591 (acc_wait_all, acc_wait_all_async): Use base_dev not ACC_dev.
592 * oacc-cuda.c (oacc-int.h): Include.
593 (acc_get_current_cuda_device, acc_get_current_cuda_context)
594 (acc_get_cuda_stream): Use base_dev not ACC_dev.
595 (acc_set_cuda_stream): Call ACC_lazy_initialize, use base_dev not
596 ACC_dev.
597 * oacc-host.c (oacc-plugin.h, oacc-int.h): Include one or the
598 other, depending on HOST_NONSHM_PLUGIN setting.
599 (openacc_create_thread_data, openacc_destroy_thread_data): New.
600 (host_dispatch): Initialize create_thread_data_func,
601 destroy_thread_data_func hooks.
602 * oacc-init.c (oacc-int.h): Include.
603 (acc_device_lock): Make static.
604 (ACC_dev, ACC_handle, handle_num, struct ACC_context, ACC_contexts):
605 Remove.
606 (base_dev, goacc_threads, goacc_thread_lock, goacc_cleanup_key):
607 Add.
608 (goacc_tls_data, goacc_tls_key): Define one or the other, depending
609 on HAVE_TLS setting.
610 (dispatchers): Add comment.
611 (ACC_register): Only register 0th device.
612 (close_handle): Remove.
613 (_acc_init): Add comment. Don't use ACC_dev.
614 (goacc_new_thread, goacc_destroy_thread): New.
615 (lazy_open): Update comment. Remove code relating to contexts and
616 memory maps. Create thread-specific data if necessary.
617 (acc_init): Use base_dev not ACC_dev.
618 (_acc_shutdown): Don't call close_handle. Use base_dev not ACC_dev.
619 Free target-specific TLS data and close devices that are open at
620 the time of shutdown.
621 (lazy_init): Add comment. Use base_dev not ACC_dev.
622 (lazy_init_and_open): Add comment. Use base_dev not ACC_dev.
623 (acc_get_num_devices, acc_get_device_type, acc_get_device_num): Use
624 base_dev not ACC_dev.
625 (acc_set_device_num): Likewise. If switching device number,
626 de-associate previous device number from the current thread, but do
627 not close the device.
628 (acc_on_device): Check type for device for current thread, not
629 ACC_dev.
630 (ACC_runtime_initialize): Initialize goacc_tls_key,
631 goacc_cleanup_key, base_dev, goacc_threads, goacc_thread_lock. Don't
632 initialize ACC_contexts.
633 (saved_bound_dev): Remove.
634 (ACC_save_and_set_bind, ACC_restore_bind): Use goacc_thread.
635 (ACC_lazy_initialize): Use base_dev, goacc_thread instead of
636 ACC_dev, ACC_memmap.
637 * oacc-int.h (struct ACC_dispatch_t): Don't declare here.
638 (struct goacc_thread): New.
639 (goacc_tls_data): Define for HAVE_TLS.
640 (goacc_tls_key): Define for !HAVE_TLS.
641 (goacc_thread): New (versions with and without HAVE_TLS).
642 (ACC_mem_open, ACC_mem_close, ACC_resolve_device, ACC_dev)
643 (ACC_handle, struct memmap_t, ACC_memmap): Remove.
644 (base_dev): Add extern declaration.
645 * oacc-mem.c (oacc-int.h, assert.h): Include.
646 (ACC_memmap, ACC_mem_open, ACC_mem_close): Remove.
647 (lookup_host): Change memmap_t argument to struct
648 gomp_memory_mapping.
649 (lookup_dev): Change memmap_t argument to struct target_mem_desc.
650 Use list_count not refcount for iterating over mapped elements.
651 (acc_malloc): Use base_dev not ACC_dev.
652 (acc_free): Update call to lookup_dev. Use base_dev not ACC_dev.
653 (acc_memcpy_to_device, acc_memcpy_from_device): Use base_dev not
654 ACC_dev.
655 (acc_deviceptr, acc_is_present): Update call to lookup_host.
656 (acc_hostptr): Update call to lookup_dev.
657 (acc_map_data): Look up thread device instead of using ACC_dev,
658 update calls to lookup_host, lookup_dev. Use data environment in
659 device descriptor.
660 (acc_unmap_data): Update call to lookup_host. Remove mapped data
661 from data environment not ACC_memmap.
662 (present_create_copy): Update call to lookup_host. Use data
663 environment instead of list in ACC_memmap.
664 (delete_copyout): Update call to lookup_host. Look up device in
665 current thread info instead of using ACC_dev.
666 (update_dev_host): Look up device in current thread info instead of
667 using ACC_dev.
668 * oacc-parallel.c (oacc-int.h): Include.
669 (struct devgeom, devgeom, dump_devaddrs): Remove.
670 (select_acc_device): Call ACC_lazy_initialize earlier.
671 (GOACC_parallel): Use device for current thread instead of ACC_dev.
672 Use memory map from current device.
673 (GOACC_data_start): Likewise. Use thread info block for mapped data.
674 (GOACC_data_end): Use thread info block for mapped data.
675 (goacc_wait): Use device for current thread instead of ACC_dev.
676 (GOACC_update): Likewise. Formatting fixes.
677 * oacc-plugin.c (ACC_plugin_register): Remove.
678 (oacc-int.h): Include.
679 (GOMP_PLUGIN_acc_thread): New.
680 * oacc-plugin.h (target.h): Don't include.
681 (ACC_plugin_register): Remove.
682 (GOMP_PLUGIN_async_unmap_vars, GOMP_PLUGIN_acc_thread): Add extern
683 declarations.
684 * plugin-nvptx.c (oacc-plugin.h): Include.
685 (current_stream, PTX_dev, PTX_devices): Remove.
686 (struct nvptx_thread): New.
687 (nvptx_thread): New function.
688 (select_stream_for_async): Locate ptx_dev in device-specific TLS
689 data instead of using TLS PTX_dev variable.
690 (PTX_init): Don't initialize PTX_devices.
691 (PTX_open_device): Remove PTX_devices list handling. Tweak context
692 initialization.
693 (PTX_close_device): Remove PTX_devices list handling. Find PTX
694 device info via function argument instead of global TLS variable.
695 (PTX_get_num_devices): Make callable when backend has not been
696 initialized.
697 (event_gc): Find PTX device info, current stream via nvptx_thread.
698 (event_add, PTX_exec, PTX_host2dev, PTX_dev2host)
699 (PTX_async_test_all, PTX_wait_all, PTX_wait_all_async)
700 (PTX_get_current_cuda_device, PTX_get_current_cuda_context)
701 (PTX_get_cuda_stream, PTX_set_cuda_stream, openacc_close_device)
702 (openacc_set_device_num, openacc_register_async_cleanup)
703 (openacc_async_set_async): Likewise.
704 (openacc_create_thread_data, openacc_destroy_thread_data): New.
705 * target.c (oacc-int.h): Include.
706 (gomp_fini_device): Split out memory-map freeing into...
707 (gomp_free_memmap): ...this new function.
708 (gomp_load_plugin_for_device): Initialize
709 openacc.create_thread_data_func, openacc.destroy_thread_data_func
710 hooks.
711 (gomp_find_available_plugins): Initialize one target_device_descr
712 per physical device.
713 * target.h (oacc-int.h): Don't include.
714 (ACC_dispatch_t): Declare here. Add data_environ, ord fields.
715 Update comment for mem_map field.
716 (gomp_free_memmap): Add prototype.
718 2014-10-28 Thomas Schwinge <thomas@codesourcery.com>
720 * testsuite/libgomp.oacc-c/c.exp (ld_library_path, ALWAYS_CFLAGS):
721 Don't refer to CUDA installation in /opt/nvidia/cuda-5.5/.
723 * oacc-init.c: Don't use <sys/queue.h>'s SLIST_*.
724 * plugin-nvptx.c: Likewise.
726 2014-10-23 Thomas Schwinge <thomas@codesourcery.com>
728 * testsuite/libgomp.oacc-c/reduction-initial-1.c: New file.
730 2014-10-20 Cesar Philippidis <cesar@codesourcery.com>
732 * (GOACC_update): Declare.
734 2014-10-20 Julian Brown <julian@codesourcery.com>
736 * oacc-host.c (openacc_register_async_cleanup): New.
737 (host_dispatch): Initialise register_async_cleanup_func entry.
738 * oacc-int.h (struct ACC_dispatch_t): Add
739 register_async_cleanup_func hook.
740 * oacc-parallel.c (GOACC_parallel): Call
741 register_async_cleanup_func hook after queuing asynchronous
742 copy-back.
743 * plugin-nvptx.c (enum PTX_event_type): Add PTX_EVT_ASYNC_CLEANUP.
744 (struct PTX_event): Remove tgt field.
745 (event_gc): Don't do async cleanup in PTX_EVT_KNL, do it in
746 PTX_EVT_ASYNC_CLEANUP instead.
747 (event_add): Remove tgt argument. Support PTX_EVT_ASYNC_CLEANUP
748 events.
749 (PTX_exec, PTX_host2dev, PTX_dev2host, PTX_wait_async)
750 (PTX_wait_all_async): Update calls to event_add.
751 (openacc_register_async_cleanup): New.
752 (PTX_async_test): Call event_gc on success path.
753 (PTX_async_test_all): Likewise.
754 * target.c (gomp_load_plugin_for_device): Initialise
755 register_async_cleanup hook.
757 2014-10-20 Julian Brown <julian@codesourcery.com>
759 * Makefile.am (AM_CPPFLAGS): Fix search path for locating
760 gomp-constants.h.
761 * Makefile.in: Regenerate.
763 2014-10-20 Julian Brown <julian@codesourcery.com>
765 * libgomp-plugin.c (gomp_plugin_*): Rename to...
766 (GOMP_PLUGIN_*): This.
767 * libgomp-plugin.h: Likewise.
768 * libgomp.map: Likewise.
769 * oacc-host.c (GOMP): Use GOMP_PLUGIN_ in macro expansion.
770 * oacc-plugin.c (gomp_plugin_*): Rename to...
771 (GOMP_PLUGIN_*): This.
772 * plugin-nvptx.c: Likewise.
774 2014-10-17 Thomas Schwinge <thomas@codesourcery.com>
775 James Norris <jnorris@codesourcery.com>
777 * libgomp.texi: Outline documentation for OpenACC.
779 2014-10-17 James Norris <jnorris@codesourcery.com>
780 Thomas Schwinge <thomas@codesourcery.com>
781 Tom de Vries <tom@codesourcery.com>
782 Cesar Philippidis <cesar@codesourcery.com>
784 * testsuite/Makefile.in: Regenerated.
785 * testsuite/lib/libgomp.exp
786 (check_effective_target_openacc_nvidia_accel_present)
787 (check_effective_target_openacc_nvidia_accel_selected): New
788 functions.
789 * testsuite/libgomp.oacc-fortran/fortran.exp: New exp file.
790 * testsuite/libgomp.oacc-fortran/*.f: New tests.
791 * testsuite/libgomp.oacc-fortran/*.f90: Likewise.
792 * testsuite/libgomp.oacc-c/c.exp: New exp file.
793 * testsuite/libgomp.oacc-c/subr.ptx: New file.
794 * testsuite/libgomp.oacc-c/subr.cu: New file.
795 * testsuite/libgomp.oacc-c/timer.h: New file.
796 * testsuite/libgomp.oacc-c/*.c: New tests.
797 * testsuite/libgomp.oacc-c++/c++.exp: New exp file.
799 2014-10-17 Nathan Sidwell <nathan@codesourcery.com>
800 James Norris <jnorris@codesourcery.com>
801 Thomas Schwinge <thomas@codesourcery.com>
802 Tom de Vries <tom@codesourcery.com>
803 Julian Brown <julian@codesourcery.com>
805 * Makefile.am (AM_CPPFLAGS): Search in ../include also.
806 (libgomp_plugin_nvptx_version_info, libgomp_plugin_nvptx_la_SOURCES)
807 (libgomp_plugin_nvptx_la_CPPFLAGS, libgomp_plugin_nvptx_la_LDFLAGS)
808 (libgomp_plugin_nvptx_la_LIBADD)
809 (libgomp_plugin_nvptx_la_LIBTOOLFLAGS): Set variables if
810 PLUGIN_NVPTX is defined.
811 (toolexeclib_LTLIBRARIES): Add nonshm-host
812 and (conditionally) nvidia plugins.
813 (libgomp_plugin_nonshm_host_version_info)
814 (libgomp_plugin_nonshm_host_la_SOURCES)
815 (libgomp_plugin_nonshm_host_la_CPPFLAGS)
816 (libgomp_plugin_nonshm_host_la_LDFLAGS)
817 (libgomp_plugin_nonshm_host_la_LIBTOOLFLAGS): Set variables.
818 (libgomp_la_SOURCES): Add oacc-parallel.c, splay-tree.c,
819 oacc-host.c, oacc-init.c, oacc-mem.c, oacc-async.c, oacc-plugin.c,
820 oacc-cuda.c, libgomp-plugin.c.
821 (nodist_libsubinclude_HEADERS): Add openacc.h,
822 ../include/gomp-constants.h.
823 * Makefile.in: Regenerate.
824 * config.h.in: Regenerate.
825 * configure.ac: Add TODOs for OpenACC in various places.
826 (CUDA_DRIVER_CPPFLAGS, CUDA_DRIVER_LDFLAGS): Initialize.
827 (--with-cuda-driver, --with-cuda-driver-include)
828 (--with-cuda-driver-lib, --enable-offload-targets): Implement new
829 options.
830 (PLUGIN_NVPTX, PLUGIN_NVPTX_CPPFLAGS, PLUGIN_NVPTX_LDFLAGS)
831 (PLUGIN_NVPTX_LIBS): Initialize variables.
832 * configure: Regenerate.
833 * env.c (target.h): Include.
834 (goacc_device_num, goacc_device_type): New globals.
835 (goacc_parse_device_num, goacc_parse_device_type): New functions.
836 (initialize_env): Parse GCC_ACC_NOTIFY, ACC_DEVICE_TYPE,
837 ACC_DEVICE_NUM environment variables.
838 * error.c (gomp_verror, gomp_vfatal, gomp_vnotify, gomp_notify):
839 New functions.
840 (gomp_fatal): Make global.
841 * libgomp.h (stdarg.h): Include.
842 (struct gomp_memory_mapping): Forward declaration.
843 (struct gomp_task_icv): Add acc_notify_var member.
844 (goacc_device_num, goacc_device_type): Add extern declarations.
845 (gomp_vnotify, gomp_notify, gomp_verror, gomp_vfatal): Add
846 prototypes.
847 (gomp_init_targets_once): Add prototype.
848 * libgomp.map (OACC_2.0): New symbol version. Add public acc_*
849 interface functions.
850 (PLUGIN_1.0): New symbol version. Add gomp plugin interface
851 functions.
852 * libgomp_g.h (GOACC_kernels, GOACC_parallel): Update prototypes.
853 (GOACC_wait): Add prototype.
854 * target.c (limits.h, stdbool.h, stdlib.h): Don't include.
855 (oacc-plugin.h, gomp-constants.h, stdio.h, assert.h): Include.
856 (splay_tree_node, splay_tree, splay_tree_key, target_mem_desc)
857 (splay_tree_key_s, enum target_type, gomp_device_descr): Don't
858 declare here.
859 (splay-tree.h): Include.
860 (target.h): Include.
861 (splay_compare): Change linkage to hidden not static.
862 (gomp_init_targets_once): New function.
863 (gomp_get_num_devices): Use above.
864 (dump_mappings): New function (for debugging).
865 (get_kind): New function.
866 (gomp_map_vars): Add gomp_memory_mapping (mm), is_openacc
867 parameters. Change KINDS to void *. Use lock from memory map
868 not device. Use macros from gomp-constants.h instead of
869 hard-coded values. Support OpenACC-specific mappings.
870 (gomp_copy_from_async): New function.
871 (gomp_unmap_vars): Add DO_COPYFROM argument. Only copy memory
872 back from device if it is true. Use lock from memory map not
873 device.
874 (gomp_update): Add mm, is_openacc args. Use lock from
875 memory map not device. Use macros from gomp-constants.h not
876 hard-coded values.
877 (gomp_register_image_for_device): Add forward
878 declaration.
879 (GOMP_offload_register): Change TARGET_DATA type to
880 void **. Check realloc result.
881 (gomp_init_device): Change linkage to hidden not static. Tweak mem
882 map location.
883 (gomp_fini_device): New function.
884 (GOMP_target): Adjust lazy initialization, check target
885 capabilities for OpenMP 4.0 support. Add locking around splay tree
886 lookup. Add new arg to gomp_unmap_vars call.
887 (GOMP_target_data): Tweak lazy initialization. Add new args to
888 gomp_map_vars, gomp_unmap_vars calls.
889 (GOMP_target_update): Tweak lazy initialization. Add new args to
890 gomp_update call.
891 (gomp_load_plugin_for_device): Initialize device_fini and
892 OpenACC-specific plugin hooks.
893 (gomp_register_images_for_device): Rename to...
894 (gomp_register_image_for_device): This, and register a single
895 device only, and only if it has not already had images registered.
896 (gomp_find_available_plugins): Rearrange to fix plugin loading and
897 initialization for OpenACC. Prefer a device with
898 TARGET_CAP_OPENMP_400 for OpenMP.
899 * target.h: New file.
900 * splay-tree.h: Move bulk of implementation to...
901 * splay-tree.c: New file.
902 * libgomp-plugin.c: New file.
903 * libgomp-plugin.h: New file.
904 * oacc-async.c: New file.
905 * oacc-cuda.c: New file.
906 * oacc-host.c: New file.
907 * oacc-init.c: New file.
908 * oacc-mem.c: New file.
909 * oacc-parallel.c: New file.
910 * oacc-plugin.c: New file.
911 * plugin-nvptx.c: New file.
912 * oacc-int.h: New file.
913 * openacc.f90: New file.
914 * openacc.h: New file.
915 * openacc_lib.h: New file.
917 2014-10-09 Thomas Schwinge <thomas@codesourcery.com>
919 * testsuite/libgomp.oacc-c/collapse-4.c: New file, moved from
920 gcc/testsuite/gcc.dg/goacc/collapse.c.
922 2014-09-23 Thomas Schwinge <thomas@codesourcery.com>
924 * libgomp.map (OACC_2.0): Add acc_on_device, acc_on_device_.
925 * fortran.c: Include "openacc.h".
926 (acc_on_device_): New function.
927 * oacc-parallel.c: Include "openacc.h".
928 (acc_on_device): New function.
929 * openacc.f90 (acc_device_kind, acc_device_none)
930 (acc_device_default, acc_device_host, acc_device_not_host): New
931 parameters.
932 (acc_on_device): New function declaration.
933 * openacc_lib.h (acc_device_kind, acc_device_none)
934 (acc_device_default, acc_device_host, acc_device_not_host): New
935 parameters.
936 (acc_on_device): New function declaration.
937 * openacc.h (acc_device_t): New enum.
938 (acc_on_device): New function declaration.
939 * testsuite/libgomp.oacc-c/acc_on_device-1.c: New file.
940 * testsuite/libgomp.oacc-fortran/acc_on_device-1-1.f90: Likewise.
941 * testsuite/libgomp.oacc-fortran/acc_on_device-1-2.f: Likewise.
942 * testsuite/libgomp.oacc-fortran/acc_on_device-1-3.f: Likewise.
944 2014-07-09 Thomas Schwinge <thomas@codesourcery.com>
945 Jakub Jelinek <jakub@redhat.com>
947 * target.c (gomp_map_vars, gomp_unmap_vars, gomp_update): Support
948 NULL mappings as well as mapping kind OMP_CLAUSE_MAP_TO_PSET.
949 Also, some code reformatting.
951 2014-06-06 Thomas Schwinge <thomas@codesourcery.com>
952 James Norris <jnorris@codesourcery.com>
954 * libgomp.map (GOACC_2.0): Add GOACC_update.
955 * oacc-parallel.c (GOACC_update): New function.
957 2014-03-18 Ilya Verbin <ilya.verbin@intel.com>
959 * libgomp.map (GOMP_4.0.1): New symbol version.
960 Add GOMP_offload_register.
961 * plugin-host.c (device_available): Replace with:
962 (get_num_devices): This.
963 (get_type): New.
964 (offload_register): Ditto.
965 (device_init): Ditto.
966 (device_get_table): Ditto.
967 (device_run): Ditto.
968 * target.c (target_type): New enum.
969 (offload_image_descr): New struct.
970 (offload_images, num_offload_images): New globals.
971 (struct gomp_device_descr): Remove device_available_func.
972 Add type, is_initialized, get_type_func, get_num_devices_func,
973 offload_register_func, device_init_func, device_get_table_func,
974 device_run_func.
975 (mapping_table): New struct.
976 (GOMP_offload_register): New function.
977 (gomp_init_device): Ditto.
978 (GOMP_target): Add device initialization and lookup for target fn.
979 (GOMP_target_data): Add device initialization.
980 (GOMP_target_update): Ditto.
981 (gomp_load_plugin_for_device): Take handles for get_type,
982 get_num_devices, offload_register, device_init, device_get_table,
983 device_run functions.
984 (gomp_register_images_for_device): New function.
985 (gomp_find_available_plugins): Add registration of offload images.
987 2014-03-18 Thomas Schwinge <thomas@codesourcery.com>
989 * libgomp_g.h (GOACC_kernels, GOACC_parallel): Add three
990 additional int arguments.
991 * oacc-parallel.c (GOACC_kernels, GOACC_parallel): Handle these.
992 * testsuite/libgomp.oacc-c/goacc_kernels.c: Adjust.
993 * testsuite/libgomp.oacc-c/goacc_parallel.c: Likewise.
995 2014-02-28 Thomas Schwinge <thomas@codesourcery.com>
997 * testsuite/libgomp.oacc-c/goacc_kernels.c: New file.
998 * testsuite/libgomp.oacc-c/kernels-1.c: Likewise.
999 * testsuite/libgomp.oacc-c/parallel-1.c: Add one missing test.
1001 * libgomp.map (GOACC_2.0): Add GOACC_kernels.
1002 * libgomp_g.h (GOACC_kernels): New prototype.
1003 * oacc-parallel.c (GOACC_kernels): New function.
1005 2014-02-21 Thomas Schwinge <thomas@codesourcery.com>
1007 * testsuite/libgomp.oacc-c/data-1.c: New file.
1009 * libgomp.map (GOACC_2.0): Add GOACC_data_end, GOACC_data_start.
1010 * libgomp_g.h (GOACC_data_start, GOACC_data_end): New prototypes.
1011 * oacc-parallel.c (GOACC_data_start, GOACC_data_end): New
1012 functions.
1014 2014-02-20 Thomas Schwinge <thomas@codesourcery.com>
1016 * target.c (gomp_load_plugin_for_device): Don't call dlcose if
1017 dlopen failed.
1019 2014-02-20 Thomas Schwinge <thomas@codesourcery.com>
1020 James Norris <jnorris@codesourcery.com>
1022 * plugin-host.c: New file.
1023 * target.c (struct gomp_device_descr): Add device_alloc_func,
1024 device_free_func, device_dev2host_func, device_host2dev_func
1025 members.
1026 (gomp_load_plugin_for_device): Load these.
1027 (gomp_map_vars, gomp_unmap_tgt, gomp_unmap_vars, gomp_update): Use
1028 these.
1029 (resolve_device, gomp_find_available_plugins): Remove ID 257 hack.
1031 2014-02-17 Ilya Verbin <ilya.verbin@intel.com>
1033 * target.c (gomp_map_vars_existing): Don't update copy_from for the
1034 existing mappings.
1036 2014-01-28 Thomas Schwinge <thomas@codesourcery.com>
1038 * testsuite/libgomp.oacc-c/parallel-1.c: Extend.
1040 2013-12-18 Thomas Schwinge <thomas@codesourcery.com>
1042 * libgomp_g.h (GOACC_parallel): Switch kinds array to unsigned
1043 short.
1044 * oacc-parallel.c (GOACC_parallel): Likewise, and catch
1045 unsupported kinds.
1047 2013-11-08 Thomas Schwinge <thomas@codesourcery.com>
1049 libgomp/
1050 * target.c (gomp_find_available_plugins): Don't skip device 257
1051 setup.
1053 2013-11-07 Thomas Schwinge <thomas@codesourcery.com>
1055 * oacc-parallel.c: New file.
1056 * Makefile.am (libgomp_la_SOURCES): Add it.
1057 * Makefile.in: Regenerate.
1058 * libgomp.map (GOACC_2.0): Add GOACC_parallel.
1059 * libgomp_g.h (GOACC_parallel): New declaration.
1060 * testsuite/libgomp.oacc-c/goacc_parallel.c: New file.
1061 * testsuite/libgomp.oacc-c/parallel-1.c: New file.
1063 * libgomp.map (GOACC_2.0): New symbol version.
1065 * openacc.f90 (openacc_version): New integer parameter.
1066 * openacc_lib.h (openacc_version): Likewise.
1067 * testsuite/libgomp.oacc-fortran/openacc_version-1.f: New file.
1068 * testsuite/libgomp.oacc-fortran/openacc_version-2.f90: Likewise.
1070 * libgomp.map (OACC_2.0): New symbol version.
1071 * Makefile.am (nodist_libsubinclude_HEADERS): Add openacc.h.
1072 (nodist_finclude_HEADERS): Add openacc_lib.h, openacc.f90,
1073 openacc.mod, and openacc_kinds.mod.
1074 (openacc_kinds.mod): New target.
1075 (%.mod): New target, generalized from omp_lib.mod.
1076 * Makefile.in: Regenerate.
1077 * openacc.f90: New file.
1078 * openacc.h: Likewise.
1079 * openacc_lib.h: Likewise.
1080 * testsuite/libgomp.oacc-c++/c++.exp: Likewise.
1081 * testsuite/libgomp.oacc-c/c.exp: Likewise.
1082 * testsuite/libgomp.oacc-c/lib-1.c: Likewise.
1083 * testsuite/libgomp.oacc-fortran/fortran.exp: Likewise.
1084 * testsuite/libgomp.oacc-fortran/lib-1.f90: Likewise.
1085 * testsuite/libgomp.oacc-fortran/lib-2.f: Likewise.
1086 * testsuite/libgomp.oacc-fortran/lib-3.f: Likewise.
1088 Backport from trunk, r204519:
1090 * testsuite/lib/libgomp.exp (libgomp_init): Don't add -fopenmp to
1091 ALWAYS_CFLAGS.
1092 * testsuite/libgomp.c++/c++.exp (ALWAYS_CFLAGS): Add -fopenmp.
1093 * testsuite/libgomp.c/c.exp (ALWAYS_CFLAGS): Likewise.
1094 * testsuite/libgomp.fortran/fortran.exp (ALWAYS_CFLAGS): Likewise.
1095 * testsuite/libgomp.graphite/graphite.exp (ALWAYS_CFLAGS):
1096 Likewise.
1098 Backport from trunk, r204518:
1100 * libgomp_g.h: Include <stddef.h> for size_t.
1102 Backport from trunk, r204517:
1104 * libgomp.spec.in: Update comment about libgomp's dependencies.
1105 * configure.ac: Likewise.
1106 * configure: Regenerate.
1108 2013-10-10 Jakub Jelinek <jakub@redhat.com>
1110 * testsuite/libgomp.c++/udr-6.C: Remove UDR + on type F.
1112 2013-10-08 Jakub Jelinek <jakub@redhat.com>
1114 * testsuite/libgomp.c/thread-limit-1.c (main): Check if
1115 cnt isn't bigger than 6 at any point in time, sleep 10ms after
1116 incrementing it and then atomically decrement.
1117 * testsuite/libgomp.c/thread-limit-2.c (main): Likewise.
1119 * libgomp.h (struct gomp_team): Add task_queued_count field.
1120 Add comments about task_{,queued_,running_}count.
1121 * team.c (gomp_new_team): Clear task_queued_count.
1122 * task.c (GOMP_task): Increment task_queued_count.
1123 (gomp_task_run_pre): Decrement task_queued_count. If it is
1124 decremented to zero, call gomp_team_barrier_clear_task_pending.
1125 (gomp_task_run_post_handle_dependers): Increment task_queued_count.
1126 (gomp_barrier_handle_tasks): Don't call
1127 gomp_team_barrier_clear_task_pending here.
1129 * testsuite/libgomp.c/udr-2.c (main): Remove unused variable i.
1130 * testsuite/libgomp.c/udr-3.c (main): Initialize i to 0.
1131 * testsuite/libgomp.c++/udr-8.C (main): Likewise.
1133 * testsuite/libgomp.c/affinity-1.c (min_cpusetsize): New variable.
1134 (pthread_getaffinity_np): Set it when setting contig_cpucount.
1135 (print_affinity): Use it for size, only use sysconf value if that is not
1136 set and if it is smaller than sizeof (cpu_set_t), use sizeof (cpu_set_t).
1138 2013-10-07 Jakub Jelinek <jakub@redhat.com>
1140 * testsuite/libgomp.c/affinity-1.c (main): Fork even if
1141 contig_cpucount is > 8.
1143 PR libgomp/58642
1144 * config/linux/proc.c: Include errno.h.
1145 (gomp_get_cpuset_size): New variable.
1146 (gomp_cpuset_popcount): Add cpusetsize argument, use it instead of
1147 gomp_cpuset_size.
1148 (gomp_init_num_threads): If CPU_ALLOC_SIZE is defined and
1149 pthread_getaffinity_np returned EINVAL, increase gomp_cpuset_size
1150 and retry. After successful pthread_getaffinity_np copy
1151 gomp_cpuset_size to gomp_get_cpuset_size and try to find out
1152 minimum gomp_cpuset_size that covers all the CPUs set in gomp_cpusetp.
1153 (get_num_procs): Pass gomp_get_cpuset_size rather than gomp_cpuset_size
1154 to pthread_getaffinity_np, adjust gomp_cpuset_popcount caller.
1155 * config/linux/proc.h (gomp_cpuset_popcount): Add cpusetsize argument.
1156 * config/linux/affinity.c (gomp_affinity_finalize_place_list,
1157 gomp_affinity_init_level): Adjust gomp_cpuset_popcount callers.
1158 * testsuite/libgomp.c/affinity-1.c (pthread_getaffinity_np): Set
1159 contig_cpucount from the first successful pthread_getaffinity_np
1160 call, rather than just first call.
1162 2013-10-04 Jakub Jelinek <jakub@redhat.com>
1164 * libgomp.h (struct gomp_task_icv): Add thread_limit_var.
1165 (gomp_thread_limit_var, gomp_remaining_threads_count,
1166 gomp_remaining_threads_lock): Remove.
1167 (gomp_managed_threads_lock): New variable.
1168 (struct gomp_thread_pool): Add threads_busy field.
1169 (gomp_free_thread): New prototype.
1170 * parallel.c (gomp_resolve_num_threads): Adjust for
1171 thread_limit now being in icv->thread_limit_var. Use
1172 UINT_MAX instead of ULONG_MAX as infinity. If not nested,
1173 just return minimum of max_num_threads and icv->thread_limit_var
1174 and if thr->thread_pool, set threads_busy to the returned value.
1175 Otherwise, don't update atomically gomp_remaining_threads_count,
1176 but instead thr->thread_pool->threads_busy.
1177 (GOMP_parallel_end): Adjust for thread_limit now being in
1178 icv->thread_limit_var. Use UINT_MAX instead of ULONG_MAX as
1179 infinity. Adjust threads_busy in the pool rather than
1180 gomp_remaining_threads_count. Remember team->nthreads and call
1181 gomp_team_end before adjusting threads_busy, if not nested
1182 afterwards, just set it to 1 non-atomically.
1183 * team.c (gomp_thread_start): Clear thr->thread_pool and
1184 thr->task before returning.
1185 (gomp_free_pool_helper): Clear thr->thread_pool and thr->task
1186 before calling pthread_exit.
1187 (gomp_free_thread): No longer static. Use
1188 gomp_managed_threads_lock instead of gomp_remaining_threads_lock.
1189 (gomp_team_start): Set thr->thread_pool->threads_busy to
1190 nthreads immediately after creating new pool. Use
1191 gomp_managed_threads_lock instead of gomp_remaining_threads_lock.
1192 (gomp_team_end): Use gomp_managed_threads_lock instead of
1193 gomp_remaining_threads_lock.
1194 (initialize_team): Don't call gomp_sem_init here.
1195 * env.c (gomp_global_icv): Initialize thread_limit_var field.
1196 (gomp_thread_limit_var, gomp_remaining_threads_count,
1197 gomp_remaining_threads_lock): Remove.
1198 (gomp_managed_threads_locks): New variable.
1199 (handle_omp_display_env): Adjust for thread_limit var being
1200 in gomp_global_icv.
1201 (initialize_env): Likewise. If user provided value is > INT_MAX,
1202 set gomp_global_icv.thread_limit_var to UINT_MAX (infinity).
1203 Initialize gomp_managed_threads_lock instead of
1204 gomp_remaining_threads_lock.
1205 (omp_get_thread_limit): Adjust for thread_limit var in
1206 icv->thread_limit_var.
1207 * target.c: Include limits.h.
1208 (resolve_device): If device_id is < -1, return NULL.
1209 (gomp_map_vars): Make sure tgt->array, tgt->to_free, tgt->tgt_start,
1210 tgt->tgt_end and k->copy_from aren't left uninitialized.
1211 (GOMP_target): Arrange for host callback to be performed in a
1212 separate initial thread and contention group, inheriting ICVs from
1213 gomp_global_icv etc.
1214 (GOMP_teams): Adjust thread_limit_var ICV.
1215 * testsuite/libgomp.c/affinity-1.c (main): Call omp_set_dynamic (0).
1216 * testsuite/libgomp.c/target-3.c: New test.
1217 * testsuite/libgomp.c/target-4.c: New test.
1218 * testsuite/libgomp.c/target-5.c: New test.
1219 * testsuite/libgomp.c/target-6.c: New test.
1220 * testsuite/libgomp.c/target-7.c: New test.
1221 * testsuite/libgomp.c/thread-limit-1.c: New test.
1222 * testsuite/libgomp.c/thread-limit-2.c: New test.
1223 * testsuite/libgomp.c/thread-limit-3.c: New test.
1225 * libgomp.h (struct gomp_team_state): Add place_partition_off
1226 and place_partition_len fields.
1227 (struct gomp_task_icv): Add bind_var field.
1228 (gomp_bind_var_list, gomp_bind_var_list_len, gomp_places_list,
1229 gomp_places_list_len): New extern decls.
1230 (struct gomp_thread): Add place field.
1231 (gomp_cpu_affinity, gomp_cpu_affinity_len): Remove.
1232 (gomp_init_thread_affinity): Add place argument.
1233 (gomp_affinity_alloc, gomp_affinity_init_place, gomp_affinity_add_cpus,
1234 gomp_affinity_remove_cpu, gomp_affinity_copy_place,
1235 gomp_affinity_same_place, gomp_affinity_finalize_place_list,
1236 gomp_affinity_init_level, gomp_affinity_print_place): New prototypes.
1237 (gomp_team_start): Add flags argument.
1238 * team.c (struct gomp_thread_start_data): Add place field.
1239 (gomp_thread_start): Initialize thr->place.
1240 (gomp_team_start): Add flags argument. Handle OpenMP 4.0 affinity.
1241 * env.c (gomp_global_icv): Initialize bind_var field.
1242 (gomp_cpu_affinity, gomp_cpu_affinity_len): Remove.
1243 (gomp_bind_var_list, gomp_bind_var_list_len, gomp_places_list,
1244 gomp_places_list_len): New variables.
1245 (parse_bind_var, parse_one_place, parse_places_var): New functions.
1246 (parse_affinity): Rewritten to construct OMP_PLACES list with unit
1247 sized places.
1248 (handle_omp_display_env): Remove proc_bind argument. Set display
1249 to true for OMP_DISPLAY_ENV=true. Print 201307 instead of 201107
1250 as _OPENMP. Enhance printing of OMP_PROC_BIND, add printing
1251 of OMP_PLACES, don't print anything for GOMP_CPU_AFFINITY.
1252 (initialize_env): Use parse_bind_var to parse OMP_PROC_BIND
1253 instead of parse_boolean. Use parse_places_var for OMP_PLACES
1254 parsing. Don't call parse_affinity if OMP_PLACES has been
1255 successfully parsed (and call gomp_init_affinity in that case).
1256 Adjust handle_omp_display_env caller.
1257 (omp_get_proc_bind): Return bind_var ICV.
1258 * config/posix/affinity.c (gomp_init_thread_affinity): Add place
1259 argument.
1260 (gomp_affinity_alloc, gomp_affinity_init_place, gomp_affinity_add_cpus,
1261 gomp_affinity_remove_cpu, gomp_affinity_copy_place,
1262 gomp_affinity_same_place, gomp_affinity_finalize_place_list,
1263 gomp_affinity_init_level, gomp_affinity_print_place): New stubs.
1264 * config/linux/proc.c (gomp_cpuset_popcount): Fix up check extern decl.
1265 (gomp_init_num_threads): If HAVE_PTHREAD_AFFINITY_NP isn't defined,
1266 fix up sizeof argument. Free and clear gomp_cpusetp if it didn't
1267 contain any logical CPUs.
1268 (get_num_procs): Check gomp_places_list instead of gomp_cpu_affinity.
1269 * config/linux/affinity.c: Include errno.h, stdio.h and string.h.
1270 (affinity_counter): Remove.
1271 (CPU_CLR_S): Define if CPU_ALLOC_SIZE is not defined.
1272 (gomp_init_affinity): Rewritten, if gomp_places_list is NULL, try
1273 silently create OMP_PLACES=threads, if it is non-NULL afterwards,
1274 bind current thread to the first place.
1275 (gomp_init_thread_affinity): Rewritten. Add place argument, just
1276 pthread_setaffinity_np to gomp_places_list[place].
1277 (gomp_affinity_alloc, gomp_affinity_init_place, gomp_affinity_add_cpus,
1278 gomp_affinity_remove_cpu, gomp_affinity_copy_place,
1279 gomp_affinity_same_place, gomp_affinity_finalize_place_list,
1280 gomp_affinity_init_level, gomp_affinity_print_place): New functions.
1281 * parallel.c (GOMP_parallel_start): Adjust gomp_team_start caller.
1282 (GOMP_parallel): Likewise, pass through flags parameter to it.
1283 * sections.c (GOMP_parallel_sections_start): Adjust gomp_team_start
1284 caller.
1285 (GOMP_parallel_sections): Likewise, pass through flags parameter to it.
1286 * loop.c (gomp_parallel_loop_start): Add flags argument, pass it through
1287 to gomp_team_start.
1288 (GOMP_parallel_loop_static_start, GOMP_parallel_loop_dynamic_start,
1289 GOMP_parallel_loop_guided_start, GOMP_parallel_loop_runtime_start):
1290 Adjust gomp_parallel_loop_start callers.
1291 (GOMP_parallel_loop_static, GOMP_parallel_loop_dynamic,
1292 GOMP_parallel_loop_guided, GOMP_parallel_loop_runtime): Likewise, pass
1293 through flags parameter to it.
1294 * testsuite/libgomp.c/affinity-1.c: New test.
1295 * testsuite/libgomp.c++/affinity-1.C: New test.
1297 2013-10-01 Jakub Jelinek <jakub@redhat.com>
1299 PR libgomp/57298
1300 * config/linux/proc.c (gomp_cpuset_size, gomp_cpusetp): New variables.
1301 (gomp_cpuset_popcount): Use CPU_COUNT_S if available, or CPU_COUNT if
1302 gomp_cpuset_size is sizeof (cpu_set_t). Use gomp_cpuset_size instead
1303 of sizeof (cpu_set_t) to determine number of iterations.
1304 (gomp_init_num_threads): Initialize gomp_cpuset_size and gomp_cpusetp
1305 here, use gomp_cpusetp instead of &cpuset and pass gomp_cpuset_size
1306 instead of sizeof (cpu_set_t) to pthread_getaffinity_np.
1307 (get_num_procs): Don't call pthread_getaffinity_np if gomp_cpusetp
1308 is NULL. Use gomp_cpusetp instead of &cpuset and pass gomp_cpuset_size
1309 instead of sizeof (cpu_set_t) to pthread_getaffinity_np.
1310 * config/linux/proc.h (gomp_cpuset_popcount): Add attribute_hidden.
1311 (gomp_cpuset_size, gomp_cpusetp): Declare.
1312 * config/linux/affinity.c (CPU_ISSET_S, CPU_ZERO_S, CPU_SET_S): Define
1313 if CPU_ALLOC_SIZE isn't defined.
1314 (gomp_init_affinity): Don't call pthread_getaffinity_np here, instead
1315 use gomp_cpusetp computed by gomp_init_num_threads. Use CPU_*_S
1316 variants of macros with gomp_cpuset_size as set size, for cpusetnew
1317 use alloca for it if CPU_ALLOC_SIZE is defined, otherwise local
1318 fixed size variable.
1319 (gomp_init_thread_affinity): Use CPU_*_S variants of macros with
1320 gomp_cpuset_size as set size, for cpuset use alloca for it if
1321 CPU_ALLOC_SIZE is defined, otherwise local fixed size variable.
1323 2013-09-27 Jakub Jelinek <jakub@redhat.com>
1325 * libgomp.h: Include stdlib.h.
1326 (struct gomp_task_depend_entry,
1327 struct gomp_dependers_vec): New types.
1328 (struct gomp_task): Add dependers, depend_hash, depend_count,
1329 num_dependees and depend fields.
1330 (struct gomp_taskgroup): Add num_children field.
1331 (gomp_finish_task): Free depend_hash if non-NULL.
1332 * libgomp_g.h (GOMP_task): Add depend argument.
1333 * hashtab.h: New file.
1334 * task.c: Include hashtab.h.
1335 (hash_entry_type): New typedef.
1336 (htab_alloc, htab_free, htab_hash, htab_eq): New inlines.
1337 (gomp_init_task): Clear dependers, depend_hash and depend_count
1338 fields.
1339 (GOMP_task): Add depend argument, handle depend clauses. Increment
1340 num_children field in taskgroup.
1341 (gomp_task_run_pre): Don't increment task_running_count here,
1342 nor clear task_pending bit.
1343 (gomp_task_run_post_handle_depend_hash,
1344 gomp_task_run_post_handle_dependers,
1345 gomp_task_run_post_handle_depend): New functions.
1346 (gomp_task_run_post_remove_parent): Clear in_taskwait before
1347 signalling corresponding semaphore.
1348 (gomp_task_run_post_remove_taskgroup): Decrement num_children
1349 field and make the decrement to 0 MEMMODEL_RELEASE operation,
1350 rather than storing NULL to taskgroup->children. Clear
1351 in_taskgroup_wait before signalling corresponding semaphore.
1352 (gomp_barrier_handle_tasks): Move task_running_count increment
1353 and task_pending bit clearing here. Call
1354 gomp_task_run_post_handle_depend. If more than one new tasks
1355 have been queued, wake other threads if needed.
1356 (GOMP_taskwait): Call gomp_task_run_post_handle_depend. If more
1357 than one new tasks have been queued, wake other threads if needed.
1358 After waiting on taskwait_sem, enter critical section again.
1359 (GOMP_taskgroup_start): Initialize num_children field.
1360 (GOMP_taskgroup_end): Check num_children instead of children
1361 before critical section. If children is NULL, but num_children
1362 is non-zero, wait on taskgroup_sem. Call
1363 gomp_task_run_post_handle_depend. If more than one new tasks have
1364 been queued, wake other threads if needed. After waiting on
1365 taskgroup_sem, enter critical section again.
1366 * testsuite/libgomp.c/depend-1.c: New test.
1367 * testsuite/libgomp.c/depend-2.c: New test.
1368 * testsuite/libgomp.c/depend-3.c: New test.
1369 * testsuite/libgomp.c/depend-4.c: New test.
1371 2013-09-26 Jakub Jelinek <jakub@redhat.com>
1373 PR libgomp/58482
1374 * testsuite/libgomp.c/simd-6.c: New test.
1375 * testsuite/libgomp.c++/simd-8.C: New test.
1377 2013-09-25 Jakub Jelinek <jakub@redhat.com>
1379 * parallel.c (GOMP_cancellation_point, GOMP_cancel): Handle
1380 GIMPLE_CANCEL_TASKGROUP cancellation.
1381 * libgomp.h (struct gomp_task): Add next_taskgroup, prev_taskgroup,
1382 taskgroup and copy_ctors_done fields.
1383 (struct gomp_taskgroup): New type.
1384 * task.c (gomp_init_task): Initialize copy_ctors_done and taskgroup
1385 fields.
1386 (GOMP_task): Don't start a new thread also if it's taskgroup has
1387 been cancelled. Set copy_ctors_done field if needed. Initialize
1388 taskgroup field. If copy_ctors_done and already cancelled, don't
1389 discard the task. If taskgroup is non-NULL, enqueue the task
1390 into taskgroup queue.
1391 (gomp_task_run_pre, gomp_task_run_post_remove_parent,
1392 gomp_task_run_post_remove_taskgroup): New inline functions.
1393 (gomp_barrier_handle_tasks, GOMP_taskwait): Use them.
1394 (GOMP_taskgroup_start, GOMP_taskgroup_end): Implement taskgroup
1395 support.
1396 * testsuite/libgomp.c++/cancel-parallel-1.C: New test.
1397 * testsuite/libgomp.c++/cancel-parallel-2.C: New test.
1398 * testsuite/libgomp.c++/cancel-parallel-3.C: New test.
1399 * testsuite/libgomp.c++/cancel-for-1.C: New test.
1400 * testsuite/libgomp.c++/cancel-for-1.C: New test.
1401 * testsuite/libgomp.c++/cancel-taskgroup-1.C: New test.
1402 * testsuite/libgomp.c++/cancel-taskgroup-2.C: New test.
1403 * testsuite/libgomp.c++/cancel-taskgroup-3.C: New test.
1404 * testsuite/libgomp.c++/cancel-test.h: New file.
1405 * testsuite/libgomp.c++/cancel-sections-1.C: New test.
1406 * testsuite/libgomp.c++/taskgroup-1.C: New test.
1407 * testsuite/libgomp.c/cancel-taskgroup-1.c: New test.
1408 * testsuite/libgomp.c/cancel-taskgroup-2.c: New test.
1409 * testsuite/libgomp.c/taskgroup-1.c: New test.
1410 * testsuite/libgomp.c/cancel-parallel-3.c (do_some_work): Use
1411 void return type.
1413 2013-09-24 Richard Henderson <rth@redhat.com>
1414 Jakub Jelinek <jakub@redhat.com>
1416 * libgomp.map (GOMP_4.0): Export GOMP_barrier_cancel,
1417 GOMP_loop_end_cancel, GOMP_sections_end_cancel.
1418 * parallel.c (GOMP_cancellation_point): Add WHICH argument, do nothing
1419 if gomp_cancel_var is false, handle workshare and parallel
1420 cancellation point, add ialias.
1421 (GOMP_cancel): Add WHICH and DO_CANCEL arguments, do nothing if
1422 gomp_cancel_var is false, call GOMP_cancellation_point if DO_CANCEL
1423 is false, handle workshare and parallel cancellation.
1424 * config/posix/bar.c (gomp_barrier_init): Clear cancellable field.
1425 (gomp_team_barrier_wait_end): Clear BAR_CANCELLED from state.
1426 Set work_share_cancelled to 0 on last thread, use __atomic_load_n.
1427 (gomp_team_barrier_wait_cancel_end, gomp_team_barrier_wait_cancel,
1428 gomp_team_barrier_cancel): New functions.
1429 * config/posix/bar.h (gomp_barrier_t): Add cancellable field.
1430 (BAR_CANCELLED): Define.
1431 (BAR_INCR): Set to 8.
1432 (gomp_team_barrier_wait_cancel, gomp_team_barrier_wait_cancel_end,
1433 gomp_team_barrier_cancel): New prototypes.
1434 (gomp_barrier_wait_start): Preserve BAR_CANCELLED bit.
1435 (gomp_barrier_wait_cancel_start, gomp_team_barrier_wait_final,
1436 gomp_team_barrier_cancelled): New inline functions.
1437 * config/linux/bar.c (gomp_team_barrier_wait_end): Clear BAR_CANCELLED
1438 from state where needed. Set work_share_cancelled to 0 on last thread.
1439 (gomp_team_barrier_wait_final, gomp_team_barrier_wait_cancel_end,
1440 gomp_team_barrier_wait_cancel, gomp_team_barrier_cancel): New
1441 functions.
1442 * config/linux/bar.h (gomp_barrier_t): Add awaited_final field.
1443 (BAR_CANCELLED): Define.
1444 (BAR_INCR): Set to 8.
1445 (gomp_barrier_init): Initialize awaited_final field.
1446 (gomp_team_barrier_wait_final, gomp_team_barrier_wait_cancel,
1447 gomp_team_barrier_wait_cancel_end, gomp_team_barrier_cancel): New
1448 prototypes.
1449 (gomp_barrier_wait_start): Preserve BAR_CANCELLED bit.
1450 (gomp_barrier_wait_cancel_start, gomp_team_barrier_wait_final_start,
1451 gomp_team_barrier_cancelled): New inline functions.
1452 * work.c (gomp_work_share_end, gomp_work_share_end_nowait): Set
1453 team->work_shares_to_free to thr->ts.work_share before calling
1454 free_work_share.
1455 (gomp_work_share_end_cancel): New function.
1456 * team.c (gomp_thread_start): Use gomp_team_barrier_wait_final
1457 instead of gomp_team_barrier_wait.
1458 (gomp_new_team): Initialize work_shares_to_free, work_share_cancelled
1459 and team_cancelled fields.
1460 (gomp_team_end): Use gomp_team_barrier_wait_final instead of
1461 gomp_team_barrier_wait. If team->team_cancelled, call
1462 gomp_fini_worshare on ws chain starting at team->work_shares_to_free
1463 rather than thr->ts.work_share.
1464 * env.c (gomp_global_icv): Initialize target_data field.
1465 (gomp_cancel_var): New global variable.
1466 (handle_omp_display_env): Print cancel-var ICV.
1467 (initialize_env): Parse OMP_CANCELLATION env var.
1468 (omp_get_cancellation): Return gomp_cancel_var.
1469 * barrier.c (GOMP_barrier_cancel): New function.
1470 * libgomp.h (gomp_cancel_var): New extern decl.
1471 (struct gomp_team): Add work_shares_to_free, work_share_cancelled
1472 and team_cancelled fields.
1473 (gomp_cancel_kind): New enum.
1474 (gomp_work_share_end_cancel): New prototype.
1475 * libgomp_g.h (GOMP_barrier_cancel, GOMP_loop_end_cancel,
1476 GOMP_sections_end_cancel): New prototypes.
1477 (GOMP_cancel, GOMP_cancellation_point): Adjust prototypes.
1478 * task.c (GOMP_task): If gomp_team_barrier_cancelled, don't
1479 queue or start new tasks.
1480 (gomp_barrier_handle_tasks): If gomp_team_barrier_cancelled,
1481 don't start any new tasks, just free all tasks.
1482 * sections.c (GOMP_sections_end_cancel): New function.
1483 * loop.c (GOMP_loop_end_cancel): New function.
1484 * testsuite/libgomp.c/cancel-parallel-1.c: New test.
1485 * testsuite/libgomp.c/cancel-parallel-2.c: New test.
1486 * testsuite/libgomp.c/cancel-parallel-3.c: New test.
1487 * testsuite/libgomp.c/cancel-for-1.c: New test.
1488 * testsuite/libgomp.c/cancel-for-2.c: New test.
1489 * testsuite/libgomp.c/cancel-sections-1.c: New test.
1491 2013-09-23 Michael Zolotukhin <michael.v.zolotukhin@intel.com>
1493 * configure.ac: Add checks for plugins support.
1494 * config.h.in: Regenerated.
1495 * configure: Regenerated.
1496 * target.c (struct target_mem_desc): Add device_descr field.
1497 (devices): New.
1498 (num_devices): New.
1499 (struct gomp_device_descr): New.
1500 (gomp_get_num_devices): Call gomp_target_init.
1501 (resolve_device): Return device_descr instead of int.
1502 (gomp_map_vars): Add devicep argument and update the function
1503 accordingly.
1504 (gomp_unmap_tgt): Likewise.
1505 (gomp_unmap_vars): Likewise.
1506 (gomp_update): Likewise.
1507 (GOMP_target): Use device_descr struct.
1508 (GOMP_target_data): Likewise.
1509 (GOMP_target_update): Likewise.
1510 (gomp_check_plugin_file_name): New.
1511 (gomp_load_plugin_for_device): New.
1512 (gomp_find_available_plugins): New.
1513 (gomp_target_init): New.
1515 2013-09-19 Jakub Jelinek <jakub@redhat.com>
1517 * libgomp_g.h (GOMP_target): Change 3rd argument to const void *.
1518 (GOMP_target_data, GOMP_target_update): Add openmp_target argument.
1519 * target.c (GOMP_target): Change fnname argument to openmp_target,
1520 with const void * type.
1521 (GOMP_target_data, GOMP_target_update): Add openmp_target argument.
1523 * testsuite/libgomp.c/simd-4.c: New test.
1524 * testsuite/libgomp.c/simd-5.c: New test.
1525 * testsuite/libgomp.c/udr-1.c: New test.
1526 * testsuite/libgomp.c/udr-2.c: New test.
1527 * testsuite/libgomp.c/udr-3.c: New test.
1528 * testsuite/libgomp.c++/udr-9.C: New test.
1530 2013-09-18 Jakub Jelinek <jakub@redhat.com>
1532 * testsuite/libgomp.c++/simd-4.C: New test.
1533 * testsuite/libgomp.c++/simd-5.C: New test.
1534 * testsuite/libgomp.c++/simd-6.C: New test.
1535 * testsuite/libgomp.c++/simd-7.C: New test.
1536 * testsuite/libgomp.c++/udr-1.C: New test.
1537 * testsuite/libgomp.c++/udr-2.C: New test.
1538 * testsuite/libgomp.c++/udr-3.C: New test.
1539 * testsuite/libgomp.c++/udr-4.C: New test.
1540 * testsuite/libgomp.c++/udr-5.C: New test.
1541 * testsuite/libgomp.c++/udr-6.C: New test.
1542 * testsuite/libgomp.c++/udr-7.C: New test.
1543 * testsuite/libgomp.c++/udr-8.C: New test.
1545 2013-09-16 Jakub Jelinek <jakub@redhat.com>
1547 * splay-tree.h: New file.
1548 * target.c: Include stdbool.h.
1549 (splay_tree_node, splay_tree, splay_tree_key): New typedefs.
1550 (struct target_mem_desc, struct splay_tree_key_s): New structures.
1551 (splay_compare): New inline function.
1552 (gomp_get_num_devices): New function.
1553 (resolve_device): Use default_device_var ICV. Add temporarily
1554 magic testing device number 257.
1555 (dev_splay_tree, dev_env_lock): New variables.
1556 (gomp_map_vars_existing, gomp_map_vars, gomp_unmap_tgt,
1557 gomp_unmap_vars, gomp_update): New functions.
1558 (GOMP_target, GOMP_target_data, GOMP_target_end_data,
1559 GOMP_target_update): Add support for magic testing device number 257.
1560 * libgomp.h (struct target_mem_desc): Forward declare.
1561 (struct gomp_task_icv): Add default_device_var and target_data.
1562 (gomp_get_num_devices): New prototype.
1563 * env.c (gomp_global_icv): Add default_device_var initializer.
1564 (parse_int): New function.
1565 (handle_omp_display_env): Print OMP_DEFAULT_DEVICE.
1566 (initialize_env): Initialize default_device_var.
1567 (omp_set_default_device): Set default_device_var ICV.
1568 (omp_get_default_device): Query default_device_var ICV.
1569 (omp_get_num_devices): Call gomp_get_num_devices.
1570 (omp_get_num_teams, omp_get_team_num, omp_is_initial_device): Add
1571 comments.
1573 2013-09-13 Jakub Jelinek <jakub@redhat.com>
1575 PR tree-optimization/58392
1576 * testsuite/libgomp.c/pr58392.c: New test.
1578 2013-09-06 Jakub Jelinek <jakub@redhat.com>
1580 * testsuite/libgomp.c/target-2.c: New test.
1581 * testsuite/libgomp.c++/target-3.C: New test.
1583 2013-09-05 Jakub Jelinek <jakub@redhat.com>
1585 * testsuite/libgomp.c++/target-2.C: New test.
1586 * testsuite/libgomp.c++/target-2-aux.cc: New file.
1588 * libgomp.map (GOMP_4.0): Add GOMP_target, GOMP_target_data,
1589 GOMP_target_end_data, GOMP_target_update and GOMP_teams.
1590 * Makefile.am (libgomp_la_SOURCES): Add target.c.
1591 * Makefile.in: Regenerated.
1592 * target.c: New file.
1593 * libgomp_g.h (GOMP_target, GOMP_target_data,
1594 GOMP_target_end_data, GOMP_target_update, GOMP_teams): New prototypes.
1595 * testsuite/libgomp.c++/for-11.C (main): Uncomment
1596 #pragma omp target teams directive.
1597 * testsuite/libgomp.c/for-3.c (main): Likewise.
1598 * testsuite/libgomp.c++/target-1.C: New test.
1599 * testsuite/libgomp.c/target-1.c: New test.
1601 2013-07-06 Jakub Jelinek <jakub@redhat.com>
1603 * testsuite/libgomp.c/for-3.c: New test.
1604 * testsuite/libgomp.c/simd-1.c: New test.
1605 * testsuite/libgomp.c/simd-2.c: New test.
1606 * testsuite/libgomp.c/simd-3.c: New test.
1608 2013-07-05 Richard Henderson <rth@redhat.com>
1610 * config/linux/bar.c (gomp_team_barrier_wait_end): Remove one more
1611 hard-coded constant.
1613 2013-07-03 Richard Henderson <rth@redhat.com>
1615 * config/linux/bar.h (BAR_TASK_PENDING, BAR_WAS_LAST,
1616 BAR_WAITING_FOR_TASK, BAR_INCR): New.
1617 (gomp_barrier_wait_start, gomp_barrier_last_thread,
1618 gomp_team_barrier_set_task_pending,
1619 gomp_team_barrier_clear_task_pending,
1620 gomp_team_barrier_set_waiting_for_tasks,
1621 gomp_team_barrier_waiting_for_tasks,
1622 gomp_team_barrier_done): Use them.
1623 * config/linux/bar.c (gomp_barrier_wait_end,
1624 gomp_barrier_wait_last, gomp_team_barrier_wait_end): Likewise.
1625 * config/posix/bar.h, config/posix/bar.c: Similarly.
1627 2013-07-03 Jakub Jelinek <jakub@redhat.com>
1629 * testsuite/libgomp.c++/atomic-14.C: Adjust for stricter atomic
1630 seq_cst parser.
1631 * testsuite/libgomp.c++/atomic-15.C: Likewise.
1632 * testsuite/libgomp.c/atomic-17.c: Likewise.
1634 2013-06-28 Jakub Jelinek <jakub@redhat.com>
1636 * testsuite/libgomp.c++/simd-1.C: New test.
1637 * testsuite/libgomp.c++/simd-2.C: New test.
1638 * testsuite/libgomp.c++/simd-3.C: New test.
1640 2013-06-21 Jakub Jelinek <jakub@redhat.com>
1642 * testsuite/libgomp.c/for-1.h: New file.
1643 * testsuite/libgomp.c/for-2.h: New file.
1644 * testsuite/libgomp.c/for-1.c: New test.
1645 * testsuite/libgomp.c/for-2.c: New test.
1646 * testsuite/libgomp.c++/for-9.C: New test.
1647 * testsuite/libgomp.c++/for-10.C: New test.
1648 * testsuite/libgomp.c++/for-11.C: New test.
1650 2013-06-12 Jakub Jelinek <jakub@redhat.com>
1652 * fortran.c (omp_is_initial_device): Add ialias_redirect.
1653 (omp_is_initial_device_): New function.
1654 * omp_lib.f90.in (omp_is_initial_device): New interface.
1655 * omp.h.in (omp_is_initial_device): New prototype.
1656 * libgomp.map (omp_is_initial_device, omp_is_initial_device_):
1657 Export @@OMP_4.0.
1658 * env.c (omp_is_initial_device): New function. Add ialias for it.
1659 * omp_lib.h.in (omp_is_initial_device): New external.
1661 * omp_lib.f90.in (omp_get_dynamic, omp_get_nested,
1662 omp_in_parallel, omp_get_max_threads, omp_get_num_procs,
1663 omp_get_num_threads, omp_get_thread_num, omp_get_thread_limit,
1664 omp_set_max_active_levels, omp_get_max_active_levels,
1665 omp_get_level, omp_get_ancestor_thread_num,
1666 omp_get_team_size, omp_get_active_level, omp_in_final,
1667 omp_get_cancellation, omp_get_default_device,
1668 omp_get_num_devices, omp_get_num_teams, omp_get_team_num): Remove
1669 useless use omp_lib_kinds.
1671 2013-04-30 Jakub Jelinek <jakub@redhat.com>
1673 * testsuite/libgomp.c/atomic-17.c: New test.
1674 * testsuite/libgomp.c++/atomic-14.C: New test.
1675 * testsuite/libgomp.c++/atomic-15.C: New test.
1677 2013-04-10 Jakub Jelinek <jakub@redhat.com>
1679 * libgomp.map (omp_get_cancellation, omp_get_cancellation_,
1680 omp_get_proc_bind, omp_get_proc_bind_, omp_set_default_device,
1681 omp_set_default_device_, omp_set_default_device_8_,
1682 omp_get_default_device, omp_get_default_device_,
1683 omp_get_num_devices, omp_get_num_devices_, omp_get_num_teams,
1684 omp_get_num_teams_, omp_get_team_num, omp_get_team_num_): Export
1685 @@OMP_4.0.
1686 (GOMP_cancel, GOMP_cancellation_point, GOMP_parallel_loop_dynamic,
1687 GOMP_parallel_loop_guided, GOMP_parallel_loop_runtime,
1688 GOMP_parallel_loop_static, GOMP_parallel_sections, GOMP_parallel,
1689 GOMP_taskgroup_start, GOMP_taskgroup_end): Export @@GOMP_4.0.
1690 * parallel.c (GOMP_parallel_end): Add ialias.
1691 (GOMP_parallel, GOMP_cancel, GOMP_cancellation_point): New
1692 functions.
1693 * omp.h.in (omp_proc_bind_t): New typedef.
1694 (omp_get_cancellation, omp_get_proc_bind, omp_set_default_device,
1695 omp_get_default_device, omp_get_num_devices, omp_get_num_teams,
1696 omp_get_team_num): New prototypes.
1697 * env.c (omp_get_cancellation, omp_get_proc_bind,
1698 omp_set_default_device, omp_get_default_device, omp_get_num_devices,
1699 omp_get_num_teams, omp_get_team_num): New functions.
1700 * fortran.c (ULP, STR1, STR2, ialias_redirect): Removed.
1701 (omp_get_cancellation_, omp_get_proc_bind_, omp_set_default_device_,
1702 omp_set_default_device_8_, omp_get_default_device_,
1703 omp_get_num_devices_, omp_get_num_teams_, omp_get_team_num_): New
1704 functions.
1705 * libgomp.h (ialias_ulp, ialias_str1, ialias_str2, ialias_redirect,
1706 ialias_call): Define.
1707 * libgomp_g.h (GOMP_parallel_loop_static, GOMP_parallel_loop_dynamic,
1708 GOMP_parallel_loop_guided, GOMP_parallel_loop_runtime, GOMP_parallel,
1709 GOMP_cancel, GOMP_cancellation_point, GOMP_taskgroup_start,
1710 GOMP_taskgroup_end, GOMP_parallel_sections): New prototypes.
1711 * task.c (GOMP_taskgroup_start, GOMP_taskgroup_end): New functions.
1712 * sections.c (GOMP_parallel_sections): New function.
1713 * loop.c (GOMP_parallel_loop_static, GOMP_parallel_loop_dynamic,
1714 GOMP_parallel_loop_guided, GOMP_parallel_loop_runtime): New
1715 functions.
1716 (GOMP_parallel_end): Add ialias_redirect.
1717 * omp_lib.f90.in (omp_proc_bind_kind, omp_proc_bind_false,
1718 omp_proc_bind_true, omp_proc_bind_master, omp_proc_bind_close,
1719 omp_proc_bind_spread): New params.
1720 (omp_get_cancellation, omp_get_proc_bind, omp_set_default_device,
1721 omp_get_default_device, omp_get_num_devices, omp_get_num_teams,
1722 omp_get_team_num): New interfaces.
1723 * omp_lib.h.in (omp_proc_bind_kind, omp_proc_bind_false,
1724 omp_proc_bind_true, omp_proc_bind_master, omp_proc_bind_close,
1725 omp_proc_bind_spread): New params.
1726 (omp_get_cancellation, omp_get_proc_bind, omp_set_default_device,
1727 omp_get_default_device, omp_get_num_devices, omp_get_num_teams,
1728 omp_get_team_num): New externals.
1730 2013-03-20 Tobias Burnus <burnus@net-b.de>
1732 * libgomp.texi (Environment Variables): Minor cleanup,
1733 update section refs to OpenMP 4.0rc2.
1734 (OMP_DISPLAY_ENV, GOMP_SPINCOUNT): Document these
1735 environment variables.
1737 2013-03-20 Tobias Burnus <burnus@net-b.de>
1739 * env.c (handle_omp_display_env): New function.
1740 (initialize_env): Use it.
1742 2013-03-20 Jakub Jelinek <jakub@redhat.com>
1744 * testsuite/libgomp.c/atomic-14.c: Add parens to make it valid.
1745 * testsuite/libgomp.c/atomic-15.c: New test.
1746 * testsuite/libgomp.c/atomic-16.c: New test.
1748 * testsuite/libgomp.c++/atomic-10.C: New test.
1749 * testsuite/libgomp.c++/atomic-11.C: New test.
1750 * testsuite/libgomp.c++/atomic-12.C: New test.
1751 * testsuite/libgomp.c++/atomic-13.C: New test.
1752 \f
1753 Copyright (C) 2013-2014 Free Software Foundation, Inc.
1755 Copying and distribution of this file, with or without modification,
1756 are permitted in any medium without royalty provided the copyright
1757 notice and this notice are preserved.