1. 30 May, 2019 1 commit
    • gimplify.c (enum gimplify_omp_var_data): Add GOVD_CONDTEMP. · 8221c30b
      	* gimplify.c (enum gimplify_omp_var_data): Add GOVD_CONDTEMP.
      	(gimplify_adjust_omp_clauses_1): Handle GOVD_CONDTEMP.
      	(gimplify_omp_for): If worksharing loop with lastprivate conditional
      	is nested inside of parallel region, add _condtemp_ clause to both.
      	* tree-nested.c (convert_nonlocal_omp_clauses,
      	convert_local_omp_clauses): Ignore OMP_CLAUSE__CONDTEMP_ instead of
      	assertion failure.
      	* omp-general.h (struct omp_for_data): Add have_pointer_condtemp
      	member.
      	* omp-general.c (omp_extract_for_data): Compute it.
      	* omp-low.c (scan_sharing_clauses): Handle OMP_CLAUSE__CONDTEMP_.
      	(lower_rec_input_clauses): Likewise.
      	(lower_lastprivate_conditional_clauses): If OMP_CLAUSE__CONDTEMP_
      	clause is already present, just add one further one after it.
      	(lower_lastprivate_clauses): Handle cond_ptr with array type.
      	(lower_send_shared_vars): Clear _condtemp_ vars.
      	(lower_omp_1) <case GIMPLE_ASSIGN>: Handle target data like critical
      	or section or taskgroup.
      	* omp-expand.c (determine_parallel_type): Disallow combining only if
      	first OMP_CLAUSE__CONDTEMP_ has pointer type.  Disallow combining
      	of parallel sections if OMP_CLAUSE__CONDTEMP_ is present.
      	(expand_omp_for_generic, expand_omp_for_static_nochunk,
      	expand_omp_for_static_chunk, expand_omp_for): Use
      	fd->have_pointer_condtemp instead of fd->lastprivate_conditional to
      	determine if a special set of API routines are needed and if condtemp
      	needs to be initialized, while always initialize cond_var if
      	fd->lastprivate_conditional is non-zero.
      
      From-SVN: r271791
      Jakub Jelinek committed
  2. 24 May, 2019 1 commit
    • tree-core.h (enum omp_clause_code): Add OMP_CLAUSE__CONDTEMP_. · 6c7ae8c5
      	* tree-core.h (enum omp_clause_code): Add OMP_CLAUSE__CONDTEMP_.
      	* tree.h (OMP_CLAUSE_DECL): Use OMP_CLAUSE__CONDTEMP_ instead of
      	OMP_CLAUSE__REDUCTEMP_.
      	* tree.c (omp_clause_num_ops, omp_clause_code_name): Add
      	OMP_CLAUSE__CONDTEMP_.
      	(walk_tree_1): Handle OMP_CLAUSE__CONDTEMP_.
      	* tree-pretty-print.c (dump_omp_clause): Likewise.
      	* tree-nested.c (convert_nonlocal_omp_clauses,
      	convert_local_omp_clauses): Likewise.
      	* gimplify.c (enum gimplify_omp_var_data): Use hexadecimal constants
      	instead of decimal.  Add GOVD_LASTPRIVATE_CONDITIONAL.
      	(gimplify_scan_omp_clauses): Don't reject lastprivate conditional
      	on OMP_FOR.
      	(gimplify_omp_for): Warn and disable conditional modifier from
      	lastprivate on loop iterators.
      	* omp-general.h (struct omp_for_data): Add lastprivate_conditional
      	member.
      	* omp-general.c (omp_extract_for_data): Initialize it.
      	* omp-low.c (struct omp_context): Add lastprivate_conditional_map
      	member.
      	(delete_omp_context): Delete it.
      	(lower_lastprivate_conditional_clauses): New function.
      	(lower_lastprivate_clauses): Add BODY_P and CSTMT_LIST arguments,
      	handle lastprivate conditional clauses.
      	(lower_reduction_clauses): Add CLIST argument, emit it into
      	the critical section if any.
      	(lower_omp_sections): Adjust lower_lastprivate_clauses and
      	lower_reduction_clauses callers.
      	(lower_omp_for_lastprivate): Add CLIST argument, pass it through
      	to lower_lastprivate_clauses.
      	(lower_omp_for): Call lower_lastprivate_conditional_clauses, adjust
      	lower_omp_for_lastprivate and lower_reduction_clauses callers, emit
      	clist into a critical section if not emitted there already by
      	lower_reduction_clauses.
      	(lower_omp_taskreg, lower_omp_teams): Adjust lower_reduction_clauses
      	callers.
      	(lower_omp_1): Handle GIMPLE_ASSIGNs storing into lastprivate
      	conditional variables.
      	* omp-expand.c (determine_parallel_type): Punt if OMP_CLAUSE__CONDTEMP_
      	clause is present.
      	(expand_omp_for_generic, expand_omp_for_static_nochunk,
      	expand_omp_for_static_chunk): Handle lastprivate conditional.
      	(expand_omp_for): Handle fd.lastprivate_conditional like
      	fd.have_reductemp.
      gcc/testsuite/
      	* c-c++-common/gomp/lastprivate-conditional-2.c (foo): Don't expect
      	sorry for omp for.
      	* c-c++-common/gomp/lastprivate-conditional-3.c: New test.
      libgomp/
      	* testsuite/libgomp.c-c++-common/lastprivate-conditional-1.c: New test.
      	* testsuite/libgomp.c-c++-common/lastprivate-conditional-2.c: New test.
      
      From-SVN: r271610
      Jakub Jelinek committed
  3. 20 May, 2019 1 commit
    • cfgloop.h (struct loop): Add simdlen member. · f63445e5
      	* cfgloop.h (struct loop): Add simdlen member.
      	* cfgloopmanip.c (copy_loop_info): Copy simdlen as well.
      	* omp-expand.c (expand_omp_simd): Set it if simdlen clause is present.
      	* tree-vect-loop.c (vect_analyze_loop): Pass loop->simdlen != 0
      	as new argument to autovectorize_vector_sizes target hook.  If
      	loop->simdlen, pick up vector size where the vectorization factor
      	is equal to loop->simd, and if there is none, fall back to the first
      	successful one.
      	(vect_transform_loop): Adjust autovectorize_vector_sizes target hook
      	caller.
      	* omp-low.c (omp_clause_aligned_alignment): Likewise.
      	* omp-general.c (omp_max_vf): Likewise.
      	* optabs-query.c (can_vec_mask_load_store_p): Likewise.
      	* tree-vect-slp.c (vect_slp_bb): Likewise.
      	* target.def (autovectorize_vector_sizes): Add ALL argument and
      	document it.
      	* doc/tm.texi: Adjust documentation.
      	* targhooks.c (default_autovectorize_vector_sizes): Add bool argument.
      	* targhooks.h (default_autovectorize_vector_sizes): Likewise.
      	* config/aarch64/aarch64.c (aarch64_autovectorize_vector_sizes): Add
      	bool argument.
      	* config/arc/arc.c (arc_autovectorize_vector_sizes): Likewise.
      	* config/arm/arm.c (arm_autovectorize_vector_sizes): Likewise.
      	* config/mips/mips.c (mips_autovectorize_vector_sizes): Likewise.
      	* config/i386/i386.c (ix86_autovectorize_vector_sizes): Likewise.  If
      	true and TARGET_AVX512F or TARGET_AVX, push 3 or 2 sizes even if
      	preferred vector size is not 512-bit or 256-bit, just put those
      	unpreferred ones last.
      
      	* gcc.target/i386/avx512f-simd-1.c: New test.
      
      From-SVN: r271403
      Jakub Jelinek committed
  4. 17 May, 2019 2 commits
    • [PR89433] Repeated use of the C/C++ OpenACC 'routine' directive · b48f44bf
      	gcc/
      	PR middle-end/89433
      	* omp-general.c (oacc_verify_routine_clauses): Change formal
      	parameters.  Add checking if already marked with an OpenACC
      	'routine' directive.  Adjust all users.
      	gcc/c/
      	PR c/89433
      	* c-parser.c (c_finish_oacc_routine): Rework checking if already
      	marked with an OpenACC 'routine' directive.
      	gcc/cp/
      	PR c++/89433
      	* parser.c (cp_finalize_oacc_routine): Rework checking if already
      	marked with an OpenACC 'routine' directive.
      	gcc/testsuite/
      	PR testsuite/89433
      	* c-c++-common/goacc/routine-5.c: Update.
      	* c-c++-common/goacc/routine-level-of-parallelism-1.c: Likewise.
      	* c-c++-common/goacc/routine-level-of-parallelism-2.c: New file.
      
      From-SVN: r271345
      Thomas Schwinge committed
    • [PR89433] Use 'oacc_verify_routine_clauses' for C/C++ OpenACC 'routine' directives · 5bf04509
      	gcc/
      	PR middle-end/89433
      	* omp-general.c (oacc_build_routine_dims): Move some of its
      	processing into...
      	(oacc_verify_routine_clauses): ... this new function.
      	* omp-general.h (oacc_verify_routine_clauses): New prototype.
      	gcc/c/
      	PR c/89433
      	* c-parser.c (c_parser_oacc_routine): Normalize order of clauses.
      	(c_finish_oacc_routine): Call oacc_verify_routine_clauses.
      	gcc/cp/
      	PR c++/89433
      	* parser.c (cp_parser_oacc_routine)
      	(cp_parser_late_parsing_oacc_routine): Normalize order of clauses.
      	(cp_finalize_oacc_routine): Call oacc_verify_routine_clauses.
      	gcc/testsuite/
      	PR testsuite/89433
      	* c-c++-common/goacc/routine-2.c: Update, and move some test
      	into...
      	* c-c++-common/goacc/routine-level-of-parallelism-1.c: ... this
      	new file.
      
      From-SVN: r271344
      Thomas Schwinge committed
  5. 22 Feb, 2019 1 commit
    • [PR72741] Use 'oacc_build_routine_dims' for Fortran OpenACC 'routine' directives, too · 68034b1b
      ... instead of having an incomplete local implementation.
      
      With these changes in place, we can then also revert the work-around r267213
      "[nvptx] Unify C/Fortran routine handling in nvptx_goacc_validate_dims".
      
      	gcc/fortran/
      	PR fortran/72741
      	* gfortran.h (oacc_routine_lop): New enum.
      	(symbol_attribute): Use it.
      	* openmp.c (gfc_oacc_routine_dims): Replace with...
      	(gfc_oacc_routine_lop): ... this new function.
      	(gfc_match_oacc_routine): Adjust.
      	* trans-decl.c (add_attributes_to_decl): Likewise.
      	gcc/
      	PR fortran/72741
      	* omp-general.c (oacc_replace_fn_attrib): Mostly split out into...
      	(oacc_replace_fn_attrib_attr): ... this new function.
      	* omp-general.h (oacc_replace_fn_attrib_attr): New prototype.
      	* config/nvptx/nvptx.c (nvptx_goacc_validate_dims_1): Revert workaround.
      	gcc/testsuite/
      	PR fortran/72741
      	* gfortran.dg/goacc/classify-routine.f95: Adjust.
      
      Co-Authored-By: Cesar Philippidis <cesar@codesourcery.com>
      
      From-SVN: r269105
      Thomas Schwinge committed
  6. 21 Feb, 2019 1 commit
    • [omp] Move NE_EXPR handling to omp_adjust_for_condition · 031c5c8b
      2019-02-21  Martin Jambor  <mjambor@suse.cz>
      
      	PR hsa/89302
      	* omp-general.c (omp_extract_for_data): Removed a duplicate call
      	to omp_adjust_for_condition, moved NE_EXPR code_cond processing...
      	(omp_adjust_for_condition): ...here.  Added necessary parameters.
      	* omp-general.h (omp_adjust_for_condition): Updated declaration.
      	* omp-grid.c (grid_attempt_target_gridification): Adjust to pass
      	proper values to new parameters of omp_adjust_for_condition.
      
      From-SVN: r269066
      Martin Jambor committed
  7. 01 Jan, 2019 1 commit
  8. 08 Nov, 2018 1 commit
    • builtin-types.def (BT_FN_VOID_BOOL, [...]): New. · 28567c40
      	* builtin-types.def (BT_FN_VOID_BOOL, BT_FN_VOID_SIZE_SIZE_PTR,
      	BT_FN_UINT_UINT_PTR_PTR, BT_FN_UINT_OMPFN_PTR_UINT_UINT,
      	BT_FN_BOOL_UINT_LONGPTR_LONG_LONG_LONGPTR_LONGPTR_PTR_PTR,
      	BT_FN_BOOL_UINT_ULLPTR_LONG_ULL_ULLPTR_ULLPTR_PTR_PTR,
      	BT_FN_BOOL_LONG_LONG_LONG_LONG_LONG_LONGPTR_LONGPTR_PTR_PTR,
      	BT_FN_BOOL_BOOL_ULL_ULL_ULL_LONG_ULL_ULLPTR_ULLPTR_PTR_PTR): New.
      	* gengtype.c (open_base_files): Add omp-general.h.
      	* gimple.c (gimple_build_omp_critical):
      	(gimple_build_omp_taskgroup): Add CLAUSES argument.  Call
      	gimple_omp_taskgroup_set_clauses.
      	(gimple_build_omp_atomic_load): Add mo argument, call
      	gimple_omp_atomic_set_memory_order.
      	(gimple_build_omp_atomic_store): Likewise.
      	(gimple_copy): Adjust handling of GIMPLE_OMP_TASKGROUP.
      	* gimple.def (GIMPLE_OMP_TASKGROUP): Use GSS_OMP_SINGLE_LAYOUT
      	instead of GSS_OMP.
      	(GIMPLE_OMP_TEAMS): Use GSS_OMP_PARALLEL_LAYOUT instead
      	of GSS_OMP_SINGLE_LAYOUT, adjust comments.
      	* gimple.h (enum gf_mask): Add GF_OMP_TEAMS_HOST, GF_OMP_TASK_TASKWAIT
      	and GF_OMP_ATOMIC_MEMORY_ORDER.  Remove GF_OMP_ATOMIC_SEQ_CST, use
      	different value for GF_OMP_ATOMIC_NEED_VALUE.
      	(struct gimple_statement_omp_taskreg): Add GIMPLE_OMP_TEAMS to
      	comments.
      	(struct gimple_statement_omp_single_layout): And remove here.
      	(struct gomp_teams): Inherit from gimple_statement_omp_taskreg rather
      	than gimple_statement_omp_single_layout.
      	(is_a_helper <gimple_statement_omp_taskreg *>::test): Allow
      	GIMPLE_OMP_TEAMS.
      	(is_a_helper <const gimple_statement_omp_taskreg *>::test): Likewise.
      	(gimple_omp_subcode): Formatting fix.
      	(gimple_omp_teams_child_fn, gimple_omp_teams_child_fn_ptr,
      	gimple_omp_teams_set_child_fn, gimple_omp_teams_data_arg,
      	gimple_omp_teams_data_arg_ptr, gimple_omp_teams_set_data_arg,
      	gimple_omp_teams_host, gimple_omp_teams_set_host,
      	gimple_omp_task_taskwait_p, gimple_omp_task_set_taskwait_p,
      	gimple_omp_taskgroup_clauses, gimple_omp_taskgroup_clauses_ptr,
      	gimple_omp_taskgroup_set_clauses): New inline functions.
      	(gimple_build_omp_atomic_load): Add enum omp_memory_order argument.
      	(gimple_build_omp_atomic_store): Likewise.
      	(gimple_omp_atomic_seq_cst_p): Remove.
      	(gimple_omp_atomic_memory_order): New function.
      	(gimple_omp_atomic_set_seq_cst): Remove.
      	(gimple_omp_atomic_set_memory_order): New function.
      	(gimple_build_omp_taskgroup): Add clauses argument.
      	* gimple-pretty-print.c (dump_gimple_omp_taskgroup): New function.
      	(dump_gimple_omp_task): Print taskwait with depend clauses.
      	(dump_gimple_omp_atomic_load, dump_gimple_omp_atomic_store): Use
      	dump_omp_atomic_memory_order.
      	(pp_gimple_stmt_1): Handle GIMPLE_OMP_TASKGROUP.
      	* gimplify.c (enum gimplify_omp_var_data): Add GOVD_MAP_ALLOC_ONLY,
      	GOVD_MAP_FROM_ONLY and GOVD_NONTEMPORAL.
      	(enum omp_region_type): Reserve bits 1 and 2 for auxiliary flags,
      	renumber values of most of ORT_* enumerators, add ORT_HOST_TEAMS,
      	ORT_COMBINED_HOST_TEAMS, ORT_TASKGROUP, ORT_TASKLOOP and
      	ORT_UNTIED_TASKLOOP enumerators.
      	(enum gimplify_defaultmap_kind): New.
      	(struct gimplify_omp_ctx): Remove target_map_scalars_firstprivate and
      	target_map_pointers_as_0len_arrays members, add defaultmap.
      	(new_omp_context): Initialize defaultmap member.
      	(gimple_add_tmp_var): Handle ORT_TASKGROUP like ORT_WORKSHARE.
      	(maybe_fold_stmt): Don't fold even in host teams regions.
      	(omp_firstprivatize_variable): Handle ORT_TASKGROUP like
      	ORT_WORKSHARE.  Test ctx->defaultmap[GDMK_SCALAR] instead of
      	ctx->omp_firstprivatize_variable.
      	(omp_add_variable): Don't add private/firstprivate for VLAs in
      	ORT_TASKGROUP.
      	(omp_default_clause): Print "taskloop" rather than "task" if
      	ORT_*TASKLOOP.
      	(omp_notice_variable): Handle ORT_TASKGROUP like ORT_WORKSHARE.
      	Handle new defaultmap clause kinds.
      	(omp_is_private): Handle ORT_TASKGROUP like ORT_WORKSHARE.  Allow simd
      	iterator to be lastprivate or private.  Fix up diagnostics if linear
      	is used on collapse>1 simd iterator.
      	(omp_check_private): Handle ORT_TASKGROUP like ORT_WORKSHARE.
      	(gimplify_omp_depend): New function.
      	(gimplify_scan_omp_clauses): Add shared clause on parallel for
      	combined parallel master taskloop{, simd} if taskloop has
      	firstprivate, lastprivate or reduction clause.  Handle
      	OMP_CLAUSE_REDUCTION_TASK diagnostics.  Adjust tests for
      	ORT_COMBINED_TEAMS.  Gimplify depend clauses with iterators.  Handle
      	cancel and simd OMP_CLAUSE_IF_MODIFIERs.  Handle
      	OMP_CLAUSE_NONTEMPORAL.  Handle new defaultmap clause kinds.  Handle
      	OMP_CLAUSE_{TASK,IN}_REDUCTION.  Diagnose invalid conditional
      	lastprivate.
      	(gimplify_adjust_omp_clauses_1): Ignore GOVD_NONTEMPORAL.  Handle
      	GOVD_MAP_ALLOC_ONLY and GOVD_MAP_FROM_ONLY.  
      	(gimplify_adjust_omp_clauses): Handle OMP_CLAUSE_NONTEMPORAL.  Handle
      	OMP_CLAUSE_{TASK,IN}_REDUCTION.
      	(gimplify_omp_task): Handle taskwait with depend clauses.
      	(gimplify_omp_for): Add shared clause on parallel for combined
      	parallel master taskloop{, simd} if taskloop has firstprivate,
      	lastprivate or reduction clause.  Use ORT_TASKLOOP or
      	ORT_UNTIED_TASKLOOP instead of ORT_TASK or ORT_UNTIED_TASK.  Adjust
      	tests for ORT_COMBINED_TEAMS.  Handle C++ range for loops with
      	NULL TREE_PURPOSE in OMP_FOR_ORIG_DECLS.  Firstprivatize
      	__for_end and __for_range temporaries on OMP_PARALLEL for
      	distribute parallel for{, simd}.  Move OMP_CLAUSE_REDUCTION
      	and OMP_CLAUSE_IN_REDUCTION from taskloop to the task construct
      	sandwiched in between two taskloops.
      	(computable_teams_clause): Test ctx->defaultmap[GDMK_SCALAR]
      	instead of ctx->omp_firstprivatize_variable.
      	(gimplify_omp_workshare): Set ort to ORT_HOST_TEAMS or
      	ORT_COMBINED_HOST_TEAMS if not inside of target construct.  If
      	host teams, use gimplify_and_return_first etc. for body like
      	for target or target data constructs, and at the end call
      	gimple_omp_teams_set_host on the GIMPLE_OMP_TEAMS object.
      	(gimplify_omp_atomic): Use OMP_ATOMIC_MEMORY_ORDER instead
      	of OMP_ATOMIC_SEQ_CST, pass it as new argument to
      	gimple_build_omp_atomic_load and gimple_build_omp_atomic_store, remove
      	gimple_omp_atomic_set_seq_cst calls.
      	(gimplify_expr) <case OMP_TASKGROUP>: Move handling into a separate
      	case, handle taskgroup clauses.
      	* lto-streamer-out.c (hash_tree): Handle
      	OMP_CLAUSE_{TASK,IN}_REDUCTION.
      	* Makefile.in (GTFILES): Add omp-general.h.
      	* omp-builtins.def (BUILT_IN_GOMP_TASKWAIT_DEPEND,
      	BUILT_IN_GOMP_LOOP_NONMONOTONIC_RUNTIME_START,
      	BUILT_IN_GOMP_LOOP_MAYBE_NONMONOTONIC_RUNTIME_START,
      	BUILT_IN_GOMP_LOOP_START, BUILT_IN_GOMP_LOOP_ORDERED_START,
      	BUILT_IN_GOMP_LOOP_DOACROSS_START,
      	BUILT_IN_GOMP_LOOP_NONMONOTONIC_RUNTIME_NEXT,
      	BUILT_IN_GOMP_LOOP_MAYBE_NONMONOTONIC_RUNTIME_NEXT,
      	BUILT_IN_GOMP_LOOP_ULL_NONMONOTONIC_RUNTIME_START,
      	BUILT_IN_GOMP_LOOP_ULL_MAYBE_NONMONOTONIC_RUNTIME_START,
      	BUILT_IN_GOMP_LOOP_ULL_START, BUILT_IN_GOMP_LOOP_ULL_ORDERED_START,
      	BUILT_IN_GOMP_LOOP_ULL_DOACROSS_START,
      	BUILT_IN_GOMP_LOOP_ULL_NONMONOTONIC_RUNTIME_NEXT,
      	BUILT_IN_GOMP_LOOP_ULL_MAYBE_NONMONOTONIC_RUNTIME_NEXT,
      	BUILT_IN_GOMP_PARALLEL_LOOP_NONMONOTONIC_RUNTIME,
      	BUILT_IN_GOMP_PARALLEL_LOOP_MAYBE_NONMONOTONIC_RUNTIME,
      	BUILT_IN_GOMP_PARALLEL_REDUCTIONS, BUILT_IN_GOMP_SECTIONS2_START,
      	BUILT_IN_GOMP_TEAMS_REG, BUILT_IN_GOMP_TASKGROUP_REDUCTION_REGISTER,
      	BUILT_IN_GOMP_TASKGROUP_REDUCTION_UNREGISTER,
      	BUILT_IN_GOMP_TASK_REDUCTION_REMAP,
      	BUILT_IN_GOMP_WORKSHARE_TASK_REDUCTION_UNREGISTER): New builtins.
      	* omp-expand.c (workshare_safe_to_combine_p): Return false for
      	non-worksharing loops.
      	(omp_adjust_chunk_size): Don't adjust anything if chunk_size is zero.
      	(determine_parallel_type): Don't combine parallel with worksharing
      	which has _reductemp_ clause.
      	(expand_parallel_call): Emit the GOMP_*nonmonotonic_runtime* or
      	GOMP_*maybe_nonmonotonic_runtime* builtins instead of GOMP_*runtime*
      	if there is nonmonotonic modifier or if there is no modifier and no
      	ordered clause.  For dynamic and guided schedule without monotonic
      	and nonmonotonic modifier, default to nonmonotonic.
      	(expand_omp_for): Likewise.  Adjust expand_omp_for_generic caller, use
      	GOMP_loop{,_ull}{,_ordered,_doacross}_start builtins if there are
      	task reductions.
      	(expand_task_call): Add GOMP_TASK_FLAG_REDUCTION flag to flags if
      	there are any reduction clauses.
      	(expand_taskwait_call): New function.
      	(expand_teams_call): New function.
      	(expand_omp_taskreg): Allow GIMPLE_OMP_TEAMS and call
      	expand_teams_call for it.  Formatting fix.  Handle taskwait with
      	depend clauses.
      	(expand_omp_for_generic): Add SCHED_ARG argument.  Handle expansion
      	of worksharing loops with task reductions.
      	(expand_omp_for_static_nochunk, expand_omp_for_static_chunk): Handle
      	expansion of worksharing loops with task reductions.
      	(expand_omp_sections): Handle expansion of sections with task
      	reductions.
      	(expand_omp_synch): For host teams call expand_omp_taskreg.
      	(omp_memory_order_to_memmodel): New function.
      	(expand_omp_atomic_load, expand_omp_atomic_store,
      	expand_omp_atomic_fetch_op): Use it and gimple_omp_atomic_memory_order
      	instead of gimple_omp_atomic_seq_cst_p.
      	(build_omp_regions_1, omp_make_gimple_edges): Treat taskwait with
      	depend clauses as a standalone directive.
      	* omp-general.c (enum omp_requires): New variable.
      	(omp_extract_for_data): Initialize have_reductemp member.  Allow
      	NE_EXPR even in OpenMP loops, transform them into LT_EXPR or
      	GT_EXPR loops depending on incr sign.  Formatting fixes.
      	* omp-general.h (struct omp_for_data): Add have_reductemp member.
      	(enum omp_requires): New enum.
      	(omp_requires_mask): Declare.
      	* omp-grid.c (grid_eliminate_combined_simd_part): Formatting fix.
      	Fix comment typos.
      	* omp-low.c (struct omp_context): Add task_reductions and
      	task_reduction_map fields.
      	(is_host_teams_ctx): New function.
      	(is_taskreg_ctx): Return true also if is_host_teams_ctx.
      	(use_pointer_for_field): Use is_global_var instead of
      	TREE_STATIC || DECL_EXTERNAL, and apply only if not privatized
      	in outer contexts.
      	(build_outer_var_ref): Ignore taskgroup outer contexts.
      	(delete_omp_context): Release task_reductions and task_reduction_map.
      	(scan_sharing_clauses): Don't add any fields for reduction clause on
      	taskloop.  Handle OMP_CLAUSE__REDUCTEMP_.  Handle
      	OMP_CLAUSE_{IN,TASK}_REDUCTION and OMP_CLAUSE_REDUCTION with task
      	modifier.  Don't ignore shared clauses in is_host_teams_ctx contexts.
      	Handle OMP_CLAUSE_NONTEMPORAL.
      	(add_taskreg_looptemp_clauses): Add OMP_CLAUSE__REDUCTEMP_ clause if
      	needed.
      	(scan_omp_parallel): Add _reductemp_ clause if there are any reduction
      	clauses with task modifier.
      	(scan_omp_task): Handle taskwait with depend clauses.
      	(finish_taskreg_scan): Move field corresponding to _reductemp_ clause
      	first.  Move also OMP_CLAUSE__REDUCTEMP_ clause in front if present.
      	Handle GIMPLE_OMP_TEAMS like GIMPLE_OMP_PARALLEL.
      	(scan_omp_for): Fix comment formatting.
      	(scan_omp_teams): Handle host teams constructs.
      	(check_omp_nesting_restrictions): Allow teams with no outer
      	OpenMP context.  Adjust diagnostics for teams strictly nested into
      	some explicit OpenMP construct other than target.  Allow OpenMP atomics
      	inside of simd regions.
      	(scan_omp_1_stmt): Call scan_sharing_clauses for taskgroups.
      	(scan_omp_1_stmt) <case GIMPLE_OMP_TEAMS>: Temporarily bump
      	taskreg_nesting_level while scanning host teams construct.
      	(task_reduction_read): New function.
      	(lower_rec_input_clauses): Handle OMP_CLAUSE_REDUCTION on taskloop
      	construct.  Handle OMP_CLAUSE_IN_REDUCTION and OMP_CLAUSE__REDUCTEMP_
      	clauses.  Handle OMP_CLAUSE_REDUCTION with task modifier.  Remove
      	second argument create_tmp_var if it is NULL.  Don't ignore shared
      	clauses in is_host_teams_ctx contexts.  Handle
      	OMP_CLAUSE_FIRSTPRIVATE_NO_REFERENCE on OMP_CLAUSE_FIRSTPRIVATE
      	clauses.
      	(lower_reduction_clauses): Ignore reduction clauses with task
      	modifier.  Remove second argument create_tmp_var if it is NULL.
      	Initialize OMP_ATOMIC_MEMORY_ORDER to relaxed.
      	(lower_send_clauses): Ignore reduction clauses with task modifier.
      	Handle OMP_CLAUSE__REDUCTEMP_.  Don't send anything for
      	OMP_CLAUSE_REDUCTION on taskloop.  Handle OMP_CLAUSE_IN_REDUCTION.
      	(maybe_add_implicit_barrier_cancel): Add OMP_RETURN argument, don't
      	rely that it is the last stmt in body so far.  Ignore outer taskgroup
      	contexts.
      	(omp_task_reductions_find_first, omp_task_reduction_iterate,
      	lower_omp_task_reductions): New functions.
      	(lower_omp_sections): Handle reduction clauses with taskgroup
      	modifiers.  Adjust maybe_add_implicit_barrier_cancel caller.
      	(lower_omp_single): Adjust maybe_add_implicit_barrier_cancel caller.
      	(lower_omp_for): Likewise.  Handle reduction clauses with taskgroup
      	modifiers.
      	(lower_omp_taskgroup): Handle taskgroup reductions.
      	(create_task_copyfn): Copy over OMP_CLAUSE__REDUCTEMP_ pointer.
      	Handle OMP_CLAUSE_IN_REDUCTION and OMP_CLAUSE_REDUCTION clauses.
      	(lower_depend_clauses): If there are any
      	OMP_CLAUSE_DEPEND_DEPOBJ or OMP_CLAUSE_DEPEND_MUTEXINOUTSET
      	depend clauses, use a new array format.  If OMP_CLAUSE_DEPEND_LAST is
      	seen, assume lowering is done already and return early.  Set kind
      	on artificial depend clause to OMP_CLAUSE_DEPEND_LAST.
      	(lower_omp_taskreg): Handle reduction clauses with task modifier on
      	parallel construct.  Handle reduction clause on taskloop construct.
      	Handle taskwait with depend clauses.
      	(lower_omp_1): Use lower_omp_taskreg instead of lower_omp_teams
      	for host teams constructs.
      	* tree.c (omp_clause_num_ops): Add in_reduction, task_reduction,
      	nontemporal and _reductemp_ clause entries.
      	(omp_clause_code_name): Likewise.
      	(walk_tree_1): Handle OMP_CLAUSE_{IN,TASK}_REDUCTION,
      	OMP_CLAUSE_NONTEMPORAL and OMP_CLAUSE__REDUCTEMP_.
      	* tree-core.h (enum omp_clause_code): Add
      	OMP_CLAUSE_{{IN,TASK}_REDUCTION,NONTEMPORAL,_REDUCTEMP_}.
      	(enum omp_clause_defaultmap_kind, enum omp_memory_order): New.
      	(struct tree_base): Add omp_atomic_memory_order field into union.
      	Remove OMP_ATOMIC_SEQ_CST comment.
      	(enum omp_clause_depend_kind): Add OMP_CLAUSE_DEPEND_MUTEXINOUTSET
      	and OMP_CLAUSE_DEPEND_DEPOBJ.
      	(struct tree_omp_clause): Add subcode.defaultmap_kind.
      	* tree.def (OMP_TASKGROUP): Add another operand, move next to other
      	OpenMP constructs with body and clauses operands.
      	* tree.h (OMP_BODY): Use OMP_MASTER instead of OMP_TASKGROUP.
      	(OMP_CLAUSES): Use OMP_TASKGROUP instead of OMP_SINGLE.
      	(OMP_TASKGROUP_CLAUSES): Define.
      	(OMP_CLAUSE_DECL): Use OMP_CLAUSE__REDUCTEMP_ instead of
      	OMP_CLAUSE__LOOPTEMP_.
      	(OMP_ATOMIC_SEQ_CST): Remove.
      	(OMP_ATOMIC_MEMORY_ORDER, OMP_CLAUSE_FIRSTPRIVATE_NO_REFERENCE,
      	OMP_CLAUSE_LASTPRIVATE_CONDITIONAL): Define.
      	(OMP_CLAUSE_REDUCTION_CODE, OMP_CLAUSE_REDUCTION_INIT,
      	OMP_CLAUSE_REDUCTION_MERGE, OMP_CLAUSE_REDUCTION_PLACEHOLDER,
      	OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER,
      	OMP_CLAUSE_REDUCTION_OMP_ORIG_REF): Handle
      	OMP_CLAUSE_{,IN_,TASK_}REDUCTION.
      	(OMP_CLAUSE_REDUCTION_TASK, OMP_CLAUSE_REDUCTION_INSCAN,
      	OMP_CLAUSE_DEFAULTMAP_KIND, OMP_CLAUSE_DEFAULTMAP_CATEGORY,
      	OMP_CLAUSE_DEFAULTMAP_BEHAVIOR, OMP_CLAUSE_DEFAULTMAP_SET_KIND):
      	Define.
      	* tree-inline.c (remap_gimple_stmt): Remap taskgroup clauses.
      	* tree-nested.c (convert_nonlocal_omp_clauses): Handle
      	OMP_CLAUSE__REDUCTEMP_, OMP_CLAUSE_NONTEMPORAL.
      	(convert_local_omp_clauses): Likewise.  Remove useless test.
      	* tree-parloops.c (create_call_for_reduction_1): Pass
      	OMP_MEMORY_ORDER_RELAXED as new argument to
      	dump_gimple_omp_atomic_load and dump_gimple_omp_atomic_store.
      	* tree-pretty-print.c (dump_omp_iterators): New function.
      	(dump_omp_clause): Handle OMP_CLAUSE__REDUCTEMP_,
      	OMP_CLAUSE_NONTEMPORAL, OMP_CLAUSE_{TASK,IN}_REDUCTION.  Print
      	reduction modifiers.  Handle OMP_CLAUSE_DEPEND_DEPOBJ and
      	OMP_CLAUSE_DEPEND_MUTEXINOUTSET.  Print iterators in depend clauses.
      	Print __internal__ for OMP_CLAUSE_DEPEND_LAST.  Handle cancel and
      	simd OMP_CLAUSE_IF_MODIFIERs.  Handle new kinds of
      	OMP_CLAUSE_DEFAULTMAP. Print conditional: for
      	OMP_CLAUSE_LASTPRIVATE_CONDITIONAL.
      	(dump_omp_atomic_memory_order): New function.
      	(dump_generic_node): Use it.  Print taskgroup clauses.  Print
      	taskwait with depend clauses.
      	* tree-pretty-print.h (dump_omp_atomic_memory_order): Declare.
      	* tree-streamer-in.c (unpack_ts_omp_clause_value_fields):
      	Handle OMP_CLAUSE_{TASK,IN}_REDUCTION.
      	* tree-streamer-out.c (pack_ts_omp_clause_value_fields,
      	write_ts_omp_clause_tree_pointers): Likewise.
      gcc/c-family/
      	* c-common.h (c_finish_omp_taskgroup): Add CLAUSES argument.
      	(c_finish_omp_atomic): Replace bool SEQ_CST argument with
      	enum omp_memory_order MEMORY_ORDER.
      	(c_finish_omp_flush): Add MO argument.
      	(c_omp_depend_t_p, c_finish_omp_depobj): Declare.
      	(c_finish_omp_for): Add FINAL_P argument.
      	* c-omp.c: Include memmodel.h.
      	(c_finish_omp_taskgroup): Add CLAUSES argument.  Set
      	OMP_TASKGROUP_CLAUSES to it.
      	(c_finish_omp_atomic): Replace bool SEQ_CST argument with
      	enum omp_memory_order MEMORY_ORDER.  Set OMP_ATOMIC_MEMORY_ORDER
      	instead of OMP_ATOMIC_SEQ_CST.
      	(c_omp_depend_t_p, c_finish_omp_depobj): New functions.
      	(c_finish_omp_flush): Add MO argument, if not MEMMODEL_LAST, emit
      	__atomic_thread_fence call with the given value.
      	(check_omp_for_incr_expr): Formatting fixes.
      	(c_finish_omp_for): Add FINAL_P argument.  Allow NE_EXPR
      	even in OpenMP loops, diagnose if NE_EXPR and incr expression
      	is not constant expression 1 or -1.  Transform NE_EXPR loops
      	with iterators pointers to VLA into LT_EXPR or GT_EXPR loops.
      	(c_omp_check_loop_iv_r): Look for orig decl of C++ range for
      	loops too.
      	(c_omp_split_clauses): Add support for combined
      	#pragma omp parallel master and
      	#pragma omp {,parallel }master taskloop{, simd} constructs.
      	Handle OMP_CLAUSE_IN_REDUCTION.  Handle OMP_CLAUSE_REDUCTION_TASK.
      	Handle OMP_CLAUSE_NONTEMPORAL.  Handle splitting OMP_CLAUSE_IF
      	also to OMP_SIMD.  Copy OMP_CLAUSE_LASTPRIVATE_CONDITIONAL.
      	(c_omp_predetermined_sharing): Don't return
      	OMP_CLAUSE_DEFAULT_SHARED for const qualified decls.
      	* c-pragma.c (omp_pragmas): Add PRAGMA_OMP_DEPOBJ and
      	PRAGMA_OMP_REQUIRES.
      	* c-pragma.h (enum pragma_kind): Likewise.
      	(enum pragma_omp_clause): Add PRAGMA_OMP_CLAUSE_NONTEMPORAL
      	and PRAGMA_OMP_CLAUSE_{IN,TASK}_REDUCTION.
      gcc/c/
      	* c-parser.c: Include memmode.h.
      	(c_parser_omp_depobj, c_parser_omp_requires): New functions.
      	(c_parser_pragma): Handle PRAGMA_OMP_DEPOBJ and PRAGMA_OMP_REQUIRES.
      	(c_parser_omp_clause_name): Handle nontemporal, in_reduction and
      	task_reduction clauses.
      	(c_parser_omp_variable_list): Handle OMP_CLAUSE_{IN,TASK}_REDUCTION.
      	For OMP_CLAUSE_DEPEND, parse clause operands as either an array
      	section, or lvalue assignment expression.
      	(c_parser_omp_clause_if): Handle cancel and simd modifiers.
      	(c_parser_omp_clause_lastprivate): Parse optional
      	conditional: modifier.
      	(c_parser_omp_clause_hint): Require constant integer expression rather
      	than just integer expression.
      	(c_parser_omp_clause_defaultmap): Parse new kinds of defaultmap
      	clause.
      	(c_parser_omp_clause_reduction): Add IS_OMP and KIND arguments.
      	Parse reduction modifiers.  Pass KIND to c_parser_omp_variable_list.
      	(c_parser_omp_clause_nontemporal, c_parser_omp_iterators): New
      	functions.
      	(c_parser_omp_clause_depend): Parse iterator modifier and handle
      	iterators.  Parse mutexinoutset and depobj kinds.
      	(c_parser_oacc_all_clauses): Adjust c_parser_omp_clause_reduction
      	callers.
      	(c_parser_omp_all_clauses): Likewise.  Handle
      	PRAGMA_OMP_CLAUSE_NONTEMPORAL and
      	PRAGMA_OMP_CLAUSE_{IN,TASK}_REDUCTION.
      	(c_parser_omp_atomic): Parse hint and memory order clauses.  Handle
      	default memory order from requires directive if any.  Adjust
      	c_finish_omp_atomic caller.
      	(c_parser_omp_critical): Allow comma in between (name) and hint clause.
      	(c_parser_omp_flush): Parse flush with memory-order-clause.
      	(c_parser_omp_for_loop): Allow NE_EXPR even in
      	OpenMP loops, adjust c_finish_omp_for caller.
      	(OMP_SIMD_CLAUSE_MASK): Add if and nontemporal clauses.
      	(c_parser_omp_master): Add p_name, mask and cclauses arguments.
      	Allow to be called while parsing combined parallel master.
      	Parse combined master taskloop{, simd}.
      	(c_parser_omp_parallel): Parse combined
      	parallel master{, taskloop{, simd}} constructs.
      	(OMP_TASK_CLAUSE_MASK): Add in_reduction clause.
      	(OMP_TASKGROUP_CLAUSE_MASK): Define.
      	(c_parser_omp_taskgroup): Add LOC argument.  Parse taskgroup clauses.
      	(OMP_TASKWAIT_CLAUSE_MASK): Define.
      	(c_parser_omp_taskwait): Handle taskwait with depend clauses.
      	(c_parser_omp_teams): Force a BIND_EXPR with BLOCK
      	around teams body.  Use SET_EXPR_LOCATION.
      	(c_parser_omp_target_data): Allow target data
      	with only use_device_ptr clauses.
      	(c_parser_omp_target): Use SET_EXPR_LOCATION.  Set
      	OMP_REQUIRES_TARGET_USED bit in omp_requires_mask.
      	(c_parser_omp_requires): New function.
      	(c_finish_taskloop_clauses): New function.
      	(OMP_TASKLOOP_CLAUSE_MASK): Add reduction and in_reduction clauses.
      	(c_parser_omp_taskloop): Use c_finish_taskloop_clauses.  Add forward
      	declaration.  Disallow in_reduction clause when combined with parallel
      	master.
      	(c_parser_omp_construct): Adjust c_parser_omp_master and
      	c_parser_omp_taskgroup callers.
      	* c-typeck.c (c_finish_omp_cancel): Diagnose if clause with modifier
      	other than cancel.
      	(handle_omp_array_sections_1): Handle OMP_CLAUSE_{IN,TASK}_REDUCTION
      	like OMP_CLAUSE_REDUCTION.
      	(handle_omp_array_sections): Likewise.  Call save_expr on array
      	reductions before calling build_index_type.  Handle depend clauses
      	with iterators.
      	(struct c_find_omp_var_s): New type.
      	(c_find_omp_var_r, c_omp_finish_iterators): New functions.
      	(c_finish_omp_clauses): Don't diagnose nonmonotonic clause
      	with static, runtime or auto schedule kinds.  Call save_expr for whole
      	array reduction sizes.  Diagnose reductions with zero sized elements
      	or variable length structures.  Diagnose nogroup clause used with
      	reduction clause(s).  Handle depend clause with
      	OMP_CLAUSE_DEPEND_DEPOBJ.  Diagnose bit-fields.  Require
      	omp_depend_t type for OMP_CLAUSE_DEPEND_DEPOBJ kinds and
      	some different type for other kinds.  Use build_unary_op with
      	ADDR_EXPR and build_indirect_ref instead of c_mark_addressable.
      	Handle depend clauses with iterators.  Remove no longer needed special
      	case that predetermined const qualified vars may be specified in
      	firstprivate clause.  Complain if const qualified vars are mentioned
      	in data-sharing clauses other than firstprivate or shared.  Use
      	error_at with OMP_CLAUSE_LOCATION (c) as first argument instead of
      	error.  Formatting fix.  Handle OMP_CLAUSE_NONTEMPORAL and
      	OMP_CLAUSE_{IN,TASK}_REDUCTION.  Allow any lvalue as
      	OMP_CLAUSE_DEPEND operand (besides array section), adjust diagnostics.
      gcc/cp/
      	* constexpr.c (potential_constant_expression_1): Handle OMP_DEPOBJ.
      	* cp-gimplify.c (cp_genericize_r): Handle
      	OMP_CLAUSE_{IN,TASK}_REDUCTION.
      	(cxx_omp_predetermined_sharing_1): Don't return
      	OMP_CLAUSE_DEFAULT_SHARED for const qualified decls with no mutable
      	member.  Return OMP_CLAUSE_DEFAULT_FIRSTPRIVATE for this pointer.
      	* cp-objcp-common.c (cp_common_init_ts): Handle OMP_DEPOBJ.
      	* cp-tree.def (OMP_DEPOBJ): New tree code.
      	* cp-tree.h (OMP_ATOMIC_DEPENDENT_P): Return true also for first
      	argument being OMP_CLAUSE.
      	(OMP_DEPOBJ_DEPOBJ, OMP_DEPOBJ_CLAUSES): Define.
      	(cp_convert_omp_range_for, cp_finish_omp_range_for): Declare.
      	(finish_omp_atomic): Add LOC, CLAUSES and MO arguments.  Remove
      	SEQ_CST argument.
      	(finish_omp_for_block): Declare.
      	(finish_omp_flush): Add MO argument.
      	(finish_omp_depobj): Declare.
      	* cxx-pretty-print.c (cxx_pretty_printer::statement): Handle
      	OMP_DEPOBJ.
      	* dump.c (cp_dump_tree): Likewise.
      	* lex.c (cxx_init): Likewise.
      	* parser.c: Include memmodel.h.
      	(cp_parser_for): Pass false as new is_omp argument to
      	cp_parser_range_for.
      	(cp_parser_range_for): Add IS_OMP argument, return before finalizing
      	if it is true.
      	(cp_parser_omp_clause_name): Handle nontemporal, in_reduction and
      	task_reduction clauses.
              (cp_parser_omp_var_list_no_open): Handle
      	OMP_CLAUSE_{IN,TASK}_REDUCTION.  For OMP_CLAUSE_DEPEND, parse clause
      	operands as either an array section, or lvalue assignment expression.
      	(cp_parser_omp_clause_if): Handle cancel and simd modifiers.
      	(cp_parser_omp_clause_defaultmap): Parse new kinds of defaultmap
      	clause.
      	(cp_parser_omp_clause_reduction): Add IS_OMP and KIND arguments.
      	Parse reduction modifiers.  Pass KIND to c_parser_omp_variable_list.
      	(cp_parser_omp_clause_lastprivate, cp_parser_omp_iterators): New
      	functions.
      	(cp_parser_omp_clause_depend): Parse iterator modifier and handle
      	iterators.  Parse mutexinoutset and depobj kinds.
      	(cp_parser_oacc_all_clauses): Adjust cp_parser_omp_clause_reduction
      	callers.
      	(cp_parser_omp_all_clauses): Likewise.  Handle
      	PRAGMA_OMP_CLAUSE_NONTEMPORAL and
      	PRAGMA_OMP_CLAUSE_{IN,TASK}_REDUCTION.  Call
      	cp_parser_omp_clause_lastprivate for OpenMP lastprivate clause.
      	(cp_parser_omp_atomic): Pass pragma_tok->location as
      	LOC to finish_omp_atomic.  Parse hint and memory order clauses.
      	Handle default memory order from requires directive if any.  Adjust
      	finish_omp_atomic caller.
      	(cp_parser_omp_critical): Allow comma in between (name) and hint
      	clause.
      	(cp_parser_omp_depobj): New function.
      	(cp_parser_omp_flush): Parse flush with memory-order-clause.
      	(cp_parser_omp_for_cond): Allow NE_EXPR even in OpenMP loops.
      	(cp_convert_omp_range_for, cp_finish_omp_range_for): New functions.
      	(cp_parser_omp_for_loop): Parse C++11 range for loops among omp
      	loops.  Handle OMP_CLAUSE_IN_REDUCTION like OMP_CLAUSE_REDUCTION.
      	(OMP_SIMD_CLAUSE_MASK): Add if and nontemporal clauses.
      	(cp_parser_omp_simd, cp_parser_omp_for): Call keep_next_level before
      	begin_omp_structured_block and call finish_omp_for_block on
      	finish_omp_structured_block result.
      	(cp_parser_omp_master): Add p_name, mask and cclauses arguments.
      	Allow to be called while parsing combined parallel master.
      	Parse combined master taskloop{, simd}.
      	(cp_parser_omp_parallel): Parse combined
      	parallel master{, taskloop{, simd}} constructs.
      	(cp_parser_omp_single): Use SET_EXPR_LOCATION.
      	(OMP_TASK_CLAUSE_MASK): Add in_reduction clause.
      	(OMP_TASKWAIT_CLAUSE_MASK): Define.
      	(cp_parser_omp_taskwait): Handle taskwait with depend clauses.
      	(OMP_TASKGROUP_CLAUSE_MASK): Define.
      	(cp_parser_omp_taskgroup): Parse taskgroup clauses, adjust
      	c_finish_omp_taskgroup caller.
      	(cp_parser_omp_distribute): Call keep_next_level before
      	begin_omp_structured_block and call finish_omp_for_block on
      	finish_omp_structured_block result.
      	(cp_parser_omp_teams): Force a BIND_EXPR with BLOCK around teams
      	body.
      	(cp_parser_omp_target_data): Allow target data with only
      	use_device_ptr clauses.
      	(cp_parser_omp_target): Set OMP_REQUIRES_TARGET_USED bit in
      	omp_requires_mask.
      	(cp_parser_omp_requires): New function.
      	(OMP_TASKLOOP_CLAUSE_MASK): Add reduction and in_reduction clauses.
      	(cp_parser_omp_taskloop): Add forward declaration.  Disallow
      	in_reduction clause when combined with parallel master.  Call
      	keep_next_level before begin_omp_structured_block and call
      	finish_omp_for_block on finish_omp_structured_block result.
      	(cp_parser_omp_construct): Adjust cp_parser_omp_master caller.
      	(cp_parser_pragma): Handle PRAGMA_OMP_DEPOBJ and PRAGMA_OMP_REQUIRES.
      	* pt.c (tsubst_omp_clause_decl): Add iterators_cache argument.
      	Adjust recursive calls.  Handle iterators.
      	(tsubst_omp_clauses): Handle OMP_CLAUSE_{IN,TASK}_REDUCTION and
      	OMP_CLAUSE_NONTEMPORAL.  Adjust tsubst_omp_clause_decl callers.
      	(tsubst_decomp_names):
      	(tsubst_omp_for_iterator): Change orig_declv into a reference.
      	Handle range for loops.  Move orig_declv handling after declv/initv
      	handling.
      	(tsubst_expr): Force a BIND_EXPR with BLOCK around teams body.
      	Adjust finish_omp_atomic caller.  Call keep_next_level before
      	begin_omp_structured_block.  Call cp_finish_omp_range_for for range
      	for loops and use {begin,finish}_omp_structured_block instead of
      	{push,pop}_stmt_list if there are any range for loops.  Call
      	finish_omp_for_block on finish_omp_structured_block result.
      	Handle OMP_DEPOBJ.  Handle taskwait with depend clauses.  For
      	OMP_ATOMIC call tsubst_omp_clauses on clauses if any, adjust
      	finish_omp_atomic caller.  Use OMP_ATOMIC_MEMORY_ORDER rather
      	than OMP_ATOMIC_SEQ_CST.  Handle clauses on OMP_TASKGROUP.
      	(dependent_omp_for_p): Always return true for range for loops if
      	processing_template_decl.  Return true if class type iterator
      	does not have INTEGER_CST increment.
      	* semantics.c: Include memmodel.h.
      	(handle_omp_array_sections_1): Handle OMP_CLAUSE_{IN,TASK}_REDUCTION
      	like OMP_CLAUSE_REDUCTION.
      	(handle_omp_array_sections): Likewise.  Call save_expr on array
      	reductions before calling build_index_type.  Handle depend clauses
      	with iterators.
      	(finish_omp_reduction_clause): Call save_expr for whole array
      	reduction sizes.  Don't mark OMP_CLAUSE_DECL addressable if it has
      	reference type.  Do mark decl_placeholder addressable if needed.
      	Use error_at with OMP_CLAUSE_LOCATION (c) as first argument instead
      	of error.
      	(cp_omp_finish_iterators): New function.
      	(finish_omp_clauses): Don't diagnose nonmonotonic clause with static,
      	runtime or auto schedule kinds.  Diagnose nogroup clause used with
      	reduction clause(s).  Handle depend clause with
      	OMP_CLAUSE_DEPEND_DEPOBJ.  Diagnose bit-fields.  Require
      	omp_depend_t type for OMP_CLAUSE_DEPEND_DEPOBJ kinds and
      	some different type for other kinds.  Use cp_build_addr_expr
      	and cp_build_indirect_ref instead of cxx_mark_addressable.
      	Handle depend clauses with iterators.  Only handle static data members
      	in the special case that const qualified vars may be specified in
      	firstprivate clause.  Complain if const qualified vars without mutable
      	members are mentioned in data-sharing clauses other than firstprivate
      	or shared.  Use error_at with OMP_CLAUSE_LOCATION (c) as first
      	argument instead of error.  Diagnose more than one nontemporal clause
      	refering to the same variable.  Use error_at rather than error for
      	priority and hint clause diagnostics.  Fix pasto for hint clause.
      	Diagnose hint expression that doesn't fold into INTEGER_CST.
      	Diagnose if clause with modifier other than cancel.  Handle
      	OMP_CLAUSE_{IN,TASK}_REDUCTION like OMP_CLAUSE_REDUCTION.  Allow any
      	lvalue as OMP_CLAUSE_DEPEND operand (besides array section), adjust
      	diagnostics.
      	(handle_omp_for_class_iterator): Don't create a new TREE_LIST if one
      	has been created already for range for, just fill TREE_PURPOSE and
      	TREE_VALUE.  Call cp_fully_fold on incr.
      	(finish_omp_for): Don't check cond/incr if cond is global_namespace.
      	Pass to c_omp_check_loop_iv_exprs orig_declv if non-NULL.  Don't
      	use IS_EMPTY_STMT on NULL pre_body.  Adjust c_finish_omp_for caller.
      	(finish_omp_for_block): New function.
      	(finish_omp_atomic): Add LOC argument, pass it through
      	to c_finish_omp_atomic and set it as location of OMP_ATOMIC* trees.
      	Remove SEQ_CST argument.  Add CLAUSES and MO arguments.  Adjust
      	c_finish_omp_atomic caller.  Stick clauses if any into first argument
      	of wrapping OMP_ATOMIC.
      	(finish_omp_depobj): New function.
      	(finish_omp_flush): Add MO argument, if not
      	MEMMODEL_LAST, emit __atomic_thread_fence call with the given value.
      	(finish_omp_cancel): Diagnose if clause with modifier other than
      	cancel.
      gcc/fortran/
      	* trans-openmp.c (gfc_trans_omp_clauses): Use
      	OMP_CLAUSE_DEFAULTMAP_SET_KIND.
      	(gfc_trans_omp_atomic): Set OMP_ATOMIC_MEMORY_ORDER
      	rather than OMP_ATOMIC_SEQ_CST.
      	(gfc_trans_omp_taskgroup): Build OMP_TASKGROUP using
      	make_node instead of build1_loc.
      	* types.def (BT_FN_VOID_BOOL, BT_FN_VOID_SIZE_SIZE_PTR,
      	BT_FN_UINT_UINT_PTR_PTR, BT_FN_UINT_OMPFN_PTR_UINT_UINT,
      	BT_FN_BOOL_UINT_LONGPTR_LONG_LONG_LONGPTR_LONGPTR_PTR_PTR,
      	BT_FN_BOOL_UINT_ULLPTR_LONG_ULL_ULLPTR_ULLPTR_PTR_PTR,
      	BT_FN_BOOL_LONG_LONG_LONG_LONG_LONG_LONGPTR_LONGPTR_PTR_PTR,
      	BT_FN_BOOL_BOOL_ULL_ULL_ULL_LONG_ULL_ULLPTR_ULLPTR_PTR_PTR): New.
      	(BT_FN_VOID_INT_OMPFN_SIZE_PTR_PTR_PTR_UINT_PTR_PTR): Formatting fix.
      gcc/testsuite/
      	* c-c++-common/gomp/atomic-17.c: New test.
      	* c-c++-common/gomp/atomic-18.c: New test.
      	* c-c++-common/gomp/atomic-19.c: New test.
      	* c-c++-common/gomp/atomic-20.c: New test.
      	* c-c++-common/gomp/atomic-21.c: New test.
      	* c-c++-common/gomp/atomic-22.c: New test.
      	* c-c++-common/gomp/clauses-1.c (r2): New variable.
      	(foo): Add ntm argument and test if and nontemporal clauses on
      	constructs with simd.
      	(bar): Put taskloop simd inside of taskgroup with task_reduction,
      	use in_reduction clause instead of reduction.  Add another
      	taskloop simd without nogroup clause, but with reduction clause and
      	a new in_reduction.  Add ntm and i3 arguments.  Test if and
      	nontemporal clauses on constructs with simd.  Change if clauses on
      	some constructs from specific to the particular constituents to one
      	without a modifier.  Add new tests for combined host teams and for
      	new parallel master and {,parallel }master taskloop{, simd} combined
      	constructs.
      	(baz): New function with host teams tests.
      	* gcc.dg/gomp/combined-1.c: Moved to ...
      	* c-c++-common/gomp/combined-1.c: ... here.  Adjust expected library
      	call.
      	* c-c++-common/gomp/combined-2.c: New test.
      	* c-c++-common/gomp/combined-3.c: New test.
      	* c-c++-common/gomp/critical-1.c: New test.
      	* c-c++-common/gomp/critical-2.c: New test.
      	* c-c++-common/gomp/default-1.c: New test.
      	* c-c++-common/gomp/defaultmap-1.c: New test.
      	* c-c++-common/gomp/defaultmap-2.c: New test.
      	* c-c++-common/gomp/defaultmap-3.c: New test.
      	* c-c++-common/gomp/depend-5.c: New test.
      	* c-c++-common/gomp/depend-6.c: New test.
      	* c-c++-common/gomp/depend-iterator-1.c: New test.
      	* c-c++-common/gomp/depend-iterator-2.c: New test.
      	* c-c++-common/gomp/depobj-1.c: New test.
      	* c-c++-common/gomp/flush-1.c: New test.
      	* c-c++-common/gomp/flush-2.c: New test.
      	* c-c++-common/gomp/for-1.c: New test.
      	* c-c++-common/gomp/for-2.c: New test.
      	* c-c++-common/gomp/for-3.c: New test.
      	* c-c++-common/gomp/for-4.c: New test.
      	* c-c++-common/gomp/for-5.c: New test.
      	* c-c++-common/gomp/for-6.c: New test.
      	* c-c++-common/gomp/for-7.c: New test.
      	* c-c++-common/gomp/if-1.c (foo): Add some further tests.
      	* c-c++-common/gomp/if-2.c (foo): Likewise.  Expect slightly different
      	diagnostics wording in one case.
      	* c-c++-common/gomp/if-3.c: New test.
      	* c-c++-common/gomp/master-combined-1.c: New test.
      	* c-c++-common/gomp/master-combined-2.c: New test.
      	* c-c++-common/gomp/nontemporal-1.c: New test.
      	* c-c++-common/gomp/nontemporal-2.c: New test.
      	* c-c++-common/gomp/reduction-task-1.c: New test.
      	* c-c++-common/gomp/reduction-task-2.c: New test.
      	* c-c++-common/gomp/requires-1.c: New test.
      	* c-c++-common/gomp/requires-2.c: New test.
      	* c-c++-common/gomp/requires-3.c: New test.
      	* c-c++-common/gomp/requires-4.c: New test.
      	* c-c++-common/gomp/schedule-modifiers-1.c (bar): Don't expect
      	diagnostics for nonmonotonic modifier with static, runtime or auto
      	schedule kinds.
      	* c-c++-common/gomp/simd7.c: New test.
      	* c-c++-common/gomp/target-data-1.c: New test.
      	* c-c++-common/gomp/taskloop-reduction-1.c: New test.
      	* c-c++-common/gomp/taskwait-depend-1.c: New test.
      	* c-c++-common/gomp/teams-1.c: New test.
      	* c-c++-common/gomp/teams-2.c: New test.
      	* gcc.dg/gomp/appendix-a/a.24.1.c: Update from OpenMP examples.  Add
      	shared(c) clause.
      	* gcc.dg/gomp/atomic-5.c (f1): Add another expected error.
      	* gcc.dg/gomp/clause-1.c: Adjust expected diagnostics for const
      	qualified vars without mutable member no longer being predeterined
      	shared.
      	* gcc.dg/gomp/sharing-1.c: Likewise.
      	* g++.dg/gomp/clause-3.C: Likewise.
      	* g++.dg/gomp/member-2.C: Likewise.
      	* g++.dg/gomp/predetermined-1.C: Likewise.
      	* g++.dg/gomp/private-1.C: Likewise.
      	* g++.dg/gomp/sharing-1.C: Likewise.
      	* g++.dg/gomp/sharing-2.C: Likewise.  Add a few tests with aggregate
      	const static data member without mutable elements.
      	* gcc.dg/gomp/for-4.c: Expected nonmonotonic functions in the dumps.
      	* gcc.dg/gomp/for-5.c: Likewise.
      	* gcc.dg/gomp/for-6.c: Change expected library call.
      	* gcc.dg/gomp/pr39495-2.c (foo): Don't expect errors on !=.
      	* gcc.dg/gomp/reduction-2.c: New test.
      	* gcc.dg/gomp/simd-1.c: New test.
      	* gcc.dg/gomp/teams-1.c: Adjust expected diagnostic lines.
      	* g++.dg/gomp/atomic-18.C: New test.
      	* g++.dg/gomp/atomic-19.C: New test.
      	* g++.dg/gomp/atomic-5.C (f1): Adjust expected lines of read-only
      	variable messages.  Add another expected error.
      	* g++.dg/gomp/critical-3.C: New test.
      	* g++.dg/gomp/depend-iterator-1.C: New test.
      	* g++.dg/gomp/depend-iterator-2.C: New test.
      	* g++.dg/gomp/depobj-1.C: New test.
      	* g++.dg/gomp/doacross-1.C: New test.
      	* g++.dg/gomp/for-21.C: New test.
      	* g++.dg/gomp/for-4.C: Expected nonmonotonic functions in the dumps.
      	* g++.dg/gomp/for-5.C: Likewise.
      	* g++.dg/gomp/for-6.C: Change expected library call.
      	* g++.dg/gomp/loop-4.C: New test.
      	* g++.dg/gomp/pr33372-1.C: Adjust location of the expected
      	diagnostics.
      	* g++.dg/gomp/pr33372-3.C: Likewise.
      	* g++.dg/gomp/pr39495-2.C (foo): Don't expect errors on !=.
      	* g++.dg/gomp/simd-2.C: New test.
      	* g++.dg/gomp/tpl-atomic-2.C: Adjust expected diagnostic lines.
      include/
      	* gomp-constants.h (GOMP_TASK_FLAG_REDUCTION,
      	GOMP_DEPEND_IN, GOMP_DEPEND_OUT, GOMP_DEPEND_INOUT,
      	GOMP_DEPEND_MUTEXINOUTSET): Define.
      libgomp/
      	* affinity.c (gomp_display_affinity_place): New function.
      	* affinity-fmt.c: New file.
      	* alloc.c (gomp_aligned_alloc, gomp_aligned_free): New functions.
      	* config/linux/affinity.c (gomp_display_affinity_place): New function.
      	* config/nvptx/icv-device.c (omp_get_num_teams, omp_get_team_num):
      	Move these functions to ...
      	* config/nvptx/teams.c: ... here.  New file.
      	* config/nvptx/target.c (omp_pause_resource, omp_pause_resource_all):
      	New functions.
      	* config/nvptx/team.c (gomp_team_start, gomp_pause_host): New
      	functions.
      	* configure.ac: Check for aligned_alloc, posix_memalign, memalign
      	and _aligned_malloc.
      	(HAVE_UNAME, HAVE_GETHOSTNAME, HAVE_GETPID): Add new tests.
      	* configure.tgt: Add -DUSING_INITIAL_EXEC_TLS to XCFLAGS for Linux.
      	* env.c (gomp_display_affinity_var, gomp_affinity_format_var,
      	gomp_affinity_format_len): New variables.
      	(parse_schedule): Parse monotonic and nonmonotonic modifiers in
      	OMP_SCHEDULE variable.  Set GFS_MONOTONIC for monotonic schedules.
      	(handle_omp_display_env): Display monotonic/nonmonotonic schedule
      	modifiers.  Display (non-default) chunk sizes.  Print
      	OMP_DISPLAY_AFFINITY and OMP_AFFINITY_FORMAT.
      	(initialize_env): Don't call pthread_attr_setdetachstate.  Handle
      	OMP_DISPLAY_AFFINITY and OMP_AFFINITY_FORMAT env vars.
      	* fortran.c: Include stdio.h and string.h.
      	(omp_pause_resource, omp_pause_resource_all): Add ialias_redirect.
      	(omp_get_schedule_, omp_get_schedule_8_): Mask off GFS_MONOTONIC bit.
      	(omp_set_affinity_format_, omp_get_affinity_format_,
      	omp_display_affinity_, omp_capture_affinity_, omp_pause_resource_,
      	omp_pause_resource_all_): New functions.
      	* icv.c (omp_set_schedule): Mask off omp_sched_monotonic bit in
      	switch.
      	* icv-device.c (omp_get_num_teams, omp_get_team_num): Move these
      	functions to ...
      	* teams.c: ... here.  New file.
      	* libgomp_g.h: Include gstdint.h.
      	(GOMP_loop_nonmonotonic_runtime_start,
      	GOMP_loop_maybe_nonmonotonic_runtime_start, GOMP_loop_start,
      	GOMP_loop_ordered_start, GOMP_loop_nonmonotonic_runtime_next,
      	GOMP_loop_maybe_nonmonotonic_runtime_next, GOMP_loop_doacross_start,
      	GOMP_parallel_loop_nonmonotonic_runtime,
      	GOMP_parallel_loop_maybe_nonmonotonic_runtime,
      	GOMP_loop_ull_nonmonotonic_runtime_start,
      	GOMP_loop_ull_maybe_nonmonotonic_runtime_start, GOMP_loop_ull_start,
      	GOMP_loop_ull_ordered_start, GOMP_loop_ull_nonmonotonic_runtime_next,
      	GOMP_loop_ull_maybe_nonmonotonic_runtime_next,
      	GOMP_loop_ull_doacross_start, GOMP_parallel_reductions,
      	GOMP_taskwait_depend, GOMP_taskgroup_reduction_register,
      	GOMP_taskgroup_reduction_unregister, GOMP_task_reduction_remap,
      	GOMP_workshare_task_reduction_unregister, GOMP_sections2_start,
      	GOMP_teams_reg): Declare.
      	* libgomp.h (GOMP_HAVE_EFFICIENT_ALIGNED_ALLOC): Define unless
      	gomp_aligned_alloc uses fallback implementation.
      	(gomp_aligned_alloc, gomp_aligned_free): Declare.
      	(enum gomp_schedule_type): Add GFS_MONOTONIC.
      	(struct gomp_doacross_work_share): Add extra field.
      	(struct gomp_work_share): Add task_reductions field.
      	(struct gomp_taskgroup): Add workshare and reductions fields.
      	(GOMP_NEEDS_THREAD_HANDLE): Define if needed.
      	(gomp_thread_handle): New typedef.
      	(gomp_display_affinity_place, gomp_set_affinity_format,
      	gomp_display_string, gomp_display_affinity,
      	gomp_display_affinity_thread): Declare.
      	(gomp_doacross_init, gomp_doacross_ull_init): Add size_t argument.
      	(gomp_parallel_reduction_register, gomp_workshare_taskgroup_start,
      	gomp_workshare_task_reduction_register): Declare.
      	(gomp_team_start): Add taskgroup argument.
      	(gomp_pause_host): Declare.
      	(gomp_init_work_share, gomp_work_share_start): Change bool argument
      	to size_t.
      	(gomp_thread_self, gomp_thread_to_pthread_t): New inline functions.
      	* libgomp.map (GOMP_5.0): Export GOMP_loop_start,
      	GOMP_loop_ordered_start, GOMP_loop_doacross_start,
      	GOMP_loop_ull_start, GOMP_loop_ull_ordered_start,
      	GOMP_loop_ull_doacross_start,
      	GOMP_workshare_task_reduction_unregister, GOMP_sections2_start,
      	GOMP_loop_maybe_nonmonotonic_runtime_next,
      	GOMP_loop_maybe_nonmonotonic_runtime_start,
      	GOMP_loop_nonmonotonic_runtime_next,
      	GOMP_loop_nonmonotonic_runtime_start,
      	GOMP_loop_ull_maybe_nonmonotonic_runtime_next,
      	GOMP_loop_ull_maybe_nonmonotonic_runtime_start,
      	GOMP_loop_ull_nonmonotonic_runtime_next,
      	GOMP_loop_ull_nonmonotonic_runtime_start,
      	GOMP_parallel_loop_maybe_nonmonotonic_runtime,
      	GOMP_parallel_loop_nonmonotonic_runtime, GOMP_parallel_reductions,
      	GOMP_taskgroup_reduction_register,
      	GOMP_taskgroup_reduction_unregister, GOMP_task_reduction_remap,
      	GOMP_teams_reg and GOMP_taskwait_depend.
      	(OMP_5.0): Export omp_pause_resource{,_all}{,_},
      	omp_{capture,display}_affinity{,_}, and
      	omp_[gs]et_affinity_format{,_}.
      	* loop.c: Include string.h.
      	(GOMP_loop_runtime_next): Add ialias.
      	(GOMP_taskgroup_reduction_register): Add ialias_redirect.
      	(gomp_loop_static_start, gomp_loop_dynamic_start,
      	gomp_loop_guided_start, gomp_loop_ordered_static_start,
      	gomp_loop_ordered_dynamic_start, gomp_loop_ordered_guided_start,
      	gomp_loop_doacross_static_start, gomp_loop_doacross_dynamic_start,
      	gomp_loop_doacross_guided_start): Adjust gomp_work_share_start
      	or gomp_doacross_init callers.
      	(gomp_adjust_sched, GOMP_loop_start, GOMP_loop_ordered_start,
      	GOMP_loop_doacross_start): New functions.
      	(GOMP_loop_runtime_start, GOMP_loop_ordered_runtime_start,
      	GOMP_loop_doacross_runtime_start, GOMP_parallel_loop_runtime_start):
      	Mask off GFS_MONOTONIC bit.
      	(GOMP_loop_maybe_nonmonotonic_runtime_next,
      	GOMP_loop_maybe_nonmonotonic_runtime_start,
      	GOMP_loop_nonmonotonic_runtime_next,
      	GOMP_loop_nonmonotonic_runtime_start,
      	GOMP_parallel_loop_maybe_nonmonotonic_runtime,
      	GOMP_parallel_loop_nonmonotonic_runtime): New aliases or wrapper
      	functions.
      	(gomp_parallel_loop_start): Pass NULL as taskgroup to
      	gomp_team_start.
      	* loop_ull.c: Include string.h.
      	(GOMP_loop_ull_runtime_next): Add ialias.
      	(GOMP_taskgroup_reduction_register): Add ialias_redirect.
      	(gomp_loop_ull_static_start, gomp_loop_ull_dynamic_start,
      	gomp_loop_ull_guided_start, gomp_loop_ull_ordered_static_start,
      	gomp_loop_ull_ordered_dynamic_start,
      	gomp_loop_ull_ordered_guided_start,
      	gomp_loop_ull_doacross_static_start,
      	gomp_loop_ull_doacross_dynamic_start,
      	gomp_loop_ull_doacross_guided_start): Adjust gomp_work_share_start
      	and gomp_doacross_ull_init callers.
      	(gomp_adjust_sched, GOMP_loop_ull_start, GOMP_loop_ull_ordered_start,
      	GOMP_loop_ull_doacross_start): New functions.
      	(GOMP_loop_ull_runtime_start,
      	GOMP_loop_ull_ordered_runtime_start,
      	GOMP_loop_ull_doacross_runtime_start): Mask off GFS_MONOTONIC bit.
      	(GOMP_loop_ull_maybe_nonmonotonic_runtime_next,
      	GOMP_loop_ull_maybe_nonmonotonic_runtime_start,
      	GOMP_loop_ull_nonmonotonic_runtime_next,
      	GOMP_loop_ull_nonmonotonic_runtime_start): Likewise.
      	* Makefile.am (libgomp_la_SOURCES): Add teams.c and affinity-fmt.c.
      	* omp.h.in (enum omp_sched_t): Add omp_sched_monotonic.
      	(omp_pause_resource_t, omp_depend_t): New typedefs.
      	(enum omp_lock_hint_t): Renamed to ...
      	(enum omp_sync_hint_t): ... this.  Define omp_sync_hint_*
      	enumerators using numbers and omp_lock_hint_* as their aliases.
      	(omp_lock_hint_t): New typedef.  Rename to ...
      	(omp_sync_hint_t): ... this.
      	(omp_init_lock_with_hint, omp_init_nest_lock_with_hint): Use
      	omp_sync_hint_t instead of omp_lock_hint_t.
      	(omp_pause_resource, omp_pause_resource_all, omp_set_affinity_format,
      	omp_get_affinity_format, omp_display_affinity, omp_capture_affinity):
      	Declare.
      	(omp_target_is_present, omp_target_disassociate_ptr):
      	Change first argument from void * to const void *.
      	(omp_target_memcpy, omp_target_memcpy_rect): Change second argument
      	from void * to const void *.
      	(omp_target_associate_ptr): Change first and second arguments from
      	void * to const void *.
      	* omp_lib.f90.in (omp_pause_resource_kind, omp_pause_soft,
      	omp_pause_hard): New parameters.
      	(omp_pause_resource, omp_pause_resource_all, omp_set_affinity_format,
      	omp_get_affinity_format, omp_display_affinity, omp_capture_affinity):
      	New interfaces.
      	* omp_lib.h.in (omp_pause_resource_kind, omp_pause_soft,
      	omp_pause_hard): New parameters.
      	(omp_pause_resource, omp_pause_resource_all, omp_set_affinity_format,
      	omp_get_affinity_format, omp_display_affinity, omp_capture_affinity):
      	New externals.
      	* ordered.c (gomp_doacross_init, gomp_doacross_ull_init): Add
      	EXTRA argument.  If not needed to prepare array, if extra is 0,
      	clear ws->doacross, otherwise allocate just doacross structure and
      	extra payload.  If array is needed, allocate also extra payload.
      	(GOMP_doacross_post, GOMP_doacross_wait, GOMP_doacross_ull_post,
      	GOMP_doacross_ull_wait): Handle doacross->array == NULL like
      	doacross == NULL.
      	* parallel.c (GOMP_parallel_start): Pass NULL as taskgroup to
      	gomp_team_start.
      	(GOMP_parallel): Likewise.  Formatting fix.
      	(GOMP_parallel_reductions): New function.
      	(GOMP_cancellation_point): If taskgroup has workshare
      	flag set, check cancelled of prev taskgroup if any.
      	(GOMP_cancel): If taskgroup has workshare flag set, set cancelled
      	on prev taskgroup if any.
      	* sections.c: Include string.h.
      	(GOMP_taskgroup_reduction_register): Add ialias_redirect.
      	(GOMP_sections_start): Adjust gomp_work_share_start caller.
      	(GOMP_sections2_start): New function.
      	(GOMP_parallel_sections_start, GOMP_parallel_sections):
      	Pass NULL as taskgroup to gomp_team_start.
      	* single.c (GOMP_single_start, GOMP_single_copy_start): Adjust
      	gomp_work_share_start callers.
      	* target.c (GOMP_target_update_ext, GOMP_target_enter_exit_data):
      	If taskgroup has workshare flag set, check cancelled on prev
      	taskgroup if any.  Guard all cancellation tests with
      	gomp_cancel_var test.
      	(omp_target_is_present, omp_target_disassociate_ptr):
      	Change ptr argument from void * to const void *.
      	(omp_target_memcpy): Change src argument from void * to const void *.
      	(omp_target_memcpy_rect): Likewise.
      	(omp_target_memcpy_rect_worker): Likewise.  Use const char * casts
      	instead of char * where needed.
      	(omp_target_associate_ptr): Change host_ptr and device_ptr arguments
      	from void * to const void *.
      	(omp_pause_resource, omp_pause_resource_all): New functions.
      	* task.c (gomp_task_handle_depend): Handle new depend array format
      	in addition to the old.  Handle mutexinoutset kinds the same as
      	inout for now, handle unspecified kinds.
      	(gomp_create_target_task): If taskgroup has workshare flag set, check
      	cancelled on prev taskgroup if any.  Guard all cancellation tests with
      	gomp_cancel_var test.  Handle new depend array format count in
      	addition to the old.
      	(GOMP_task): Likewise.  Adjust function comment.
      	(gomp_task_run_pre): If taskgroup has workshare flag set, check
      	cancelled on prev taskgroup if any.  Guard all cancellation tests with
      	gomp_cancel_var test.
      	(GOMP_taskwait_depend): New function.
      	(gomp_task_maybe_wait_for_dependencies): Handle new depend array
      	format in addition to the old.  Handle mutexinoutset kinds the same as
      	inout for now, handle unspecified kinds.  Fix a function comment typo.
      	(gomp_taskgroup_init): New function.
      	(GOMP_taskgroup_start): Use it.
      	(gomp_reduction_register, gomp_create_artificial_team,
      	GOMP_taskgroup_reduction_register,
      	GOMP_taskgroup_reduction_unregister, GOMP_task_reduction_remap,
      	gomp_parallel_reduction_register,
      	gomp_workshare_task_reduction_register,
      	gomp_workshare_taskgroup_start,
      	GOMP_workshare_task_reduction_unregister): New functions.
      	* taskloop.c (GOMP_taskloop): If taskgroup has workshare flag set,
      	check cancelled on prev taskgroup if any.  Guard all cancellation
      	tests with gomp_cancel_var test.  Handle GOMP_TASK_FLAG_REDUCTION flag
      	by calling GOMP_taskgroup_reduction_register.
      	* team.c (gomp_thread_attr): Remove comment.
      	(struct gomp_thread_start_data): Add handle field.
      	(gomp_thread_start): Call pthread_detach.
      	(gomp_new_team): Adjust gomp_init_work_share caller.
      	(gomp_free_pool_helper): Call pthread_detach.
      	(gomp_team_start): Add taskgroup argument, initialize implicit
      	tasks' taskgroup field to that.  Don't call
      	pthread_attr_setdetachstate.  Handle OMP_DISPLAY_AFFINITY env var.
      	(gomp_team_end): Determine nesting by thr->ts.level != 0
      	rather than thr->ts.team != NULL.
      	(gomp_pause_pool_helper, gomp_pause_host): New functions.
      	* work.c (alloc_work_share): Use gomp_aligned_alloc instead of
      	gomp_malloc if GOMP_HAVE_EFFICIENT_ALIGNED_ALLOC is defined.
      	(gomp_init_work_share): Change ORDERED argument from bool to size_t,
      	if more than 1 allocate also extra payload at the end of array.  Never
      	keep ordered_team_ids NULL, set it to inline_ordered_team_ids instead.
      	(gomp_work_share_start): Change ORDERED argument from bool to size_t,
      	return true instead of ws.
      	* Makefile.in: Regenerated.
      	* configure: Regenerated.
      	* config.h.in: Regenerated.
      	* testsuite/libgomp.c/cancel-for-2.c (foo): Use cancel modifier
      	in some cases.
      	* testsuite/libgomp.c-c++-common/cancel-parallel-1.c: New test.
      	* testsuite/libgomp.c-c++-common/cancel-taskgroup-3.c: New test.
      	* testsuite/libgomp.c-c++-common/depend-iterator-1.c: New test.
      	* testsuite/libgomp.c-c++-common/depend-iterator-2.c: New test.
      	* testsuite/libgomp.c-c++-common/depend-mutexinout-1.c: New test.
      	* testsuite/libgomp.c-c++-common/depend-mutexinout-2.c: New test.
      	* testsuite/libgomp.c-c++-common/depobj-1.c: New test.
      	* testsuite/libgomp.c-c++-common/display-affinity-1.c: New test.
      	* testsuite/libgomp.c-c++-common/for-10.c: New test.
      	* testsuite/libgomp.c-c++-common/for-11.c: New test.
      	* testsuite/libgomp.c-c++-common/for-12.c: New test.
      	* testsuite/libgomp.c-c++-common/for-13.c: New test.
      	* testsuite/libgomp.c-c++-common/for-14.c: New test.
      	* testsuite/libgomp.c-c++-common/for-15.c: New test.
      	* testsuite/libgomp.c-c++-common/for-2.h: If CONDNE macro is defined,
      	define a different N(test), don't define N(f0) to N(f14), but instead
      	define N(f20) to N(f34) using != comparisons.
      	* testsuite/libgomp.c-c++-common/for-7.c: New test.
      	* testsuite/libgomp.c-c++-common/for-8.c: New test.
      	* testsuite/libgomp.c-c++-common/for-9.c: New test.
      	* testsuite/libgomp.c-c++-common/master-combined-1.c: New test.
      	* testsuite/libgomp.c-c++-common/pause-1.c: New test.
      	* testsuite/libgomp.c-c++-common/pause-2.c: New test.
      	* testsuite/libgomp.c-c++-common/pr66199-10.c: New test.
      	* testsuite/libgomp.c-c++-common/pr66199-11.c: New test.
      	* testsuite/libgomp.c-c++-common/pr66199-12.c: New test.
      	* testsuite/libgomp.c-c++-common/pr66199-13.c: New test.
      	* testsuite/libgomp.c-c++-common/pr66199-14.c: New test.
      	* testsuite/libgomp.c-c++-common/simd-1.c: New test.
      	* testsuite/libgomp.c-c++-common/taskloop-reduction-1.c: New test.
      	* testsuite/libgomp.c-c++-common/taskloop-reduction-2.c: New test.
      	* testsuite/libgomp.c-c++-common/taskloop-reduction-3.c: New test.
      	* testsuite/libgomp.c-c++-common/taskloop-reduction-4.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-11.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-12.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-1.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-2.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-3.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-4.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-5.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-6.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-7.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-8.c: New test.
      	* testsuite/libgomp.c-c++-common/task-reduction-9.c: New test.
      	* testsuite/libgomp.c-c++-common/taskwait-depend-1.c: New test.
      	* testsuite/libgomp.c++/depend-1.C: New test.
      	* testsuite/libgomp.c++/depend-iterator-1.C: New test.
      	* testsuite/libgomp.c++/depobj-1.C: New test.
      	* testsuite/libgomp.c++/for-16.C: New test.
      	* testsuite/libgomp.c++/for-21.C: New test.
      	* testsuite/libgomp.c++/for-22.C: New test.
      	* testsuite/libgomp.c++/for-23.C: New test.
      	* testsuite/libgomp.c++/for-24.C: New test.
      	* testsuite/libgomp.c++/for-25.C: New test.
      	* testsuite/libgomp.c++/for-26.C: New test.
      	* testsuite/libgomp.c++/taskloop-reduction-1.C: New test.
      	* testsuite/libgomp.c++/taskloop-reduction-2.C: New test.
      	* testsuite/libgomp.c++/taskloop-reduction-3.C: New test.
      	* testsuite/libgomp.c++/taskloop-reduction-4.C: New test.
      	* testsuite/libgomp.c++/task-reduction-10.C: New test.
      	* testsuite/libgomp.c++/task-reduction-11.C: New test.
      	* testsuite/libgomp.c++/task-reduction-12.C: New test.
      	* testsuite/libgomp.c++/task-reduction-13.C: New test.
      	* testsuite/libgomp.c++/task-reduction-14.C: New test.
      	* testsuite/libgomp.c++/task-reduction-15.C: New test.
      	* testsuite/libgomp.c++/task-reduction-16.C: New test.
      	* testsuite/libgomp.c++/task-reduction-17.C: New test.
      	* testsuite/libgomp.c++/task-reduction-18.C: New test.
      	* testsuite/libgomp.c++/task-reduction-19.C: New test.
      	* testsuite/libgomp.c/task-reduction-1.c: New test.
      	* testsuite/libgomp.c++/task-reduction-1.C: New test.
      	* testsuite/libgomp.c/task-reduction-2.c: New test.
      	* testsuite/libgomp.c++/task-reduction-2.C: New test.
      	* testsuite/libgomp.c++/task-reduction-3.C: New test.
      	* testsuite/libgomp.c++/task-reduction-4.C: New test.
      	* testsuite/libgomp.c++/task-reduction-5.C: New test.
      	* testsuite/libgomp.c++/task-reduction-6.C: New test.
      	* testsuite/libgomp.c++/task-reduction-7.C: New test.
      	* testsuite/libgomp.c++/task-reduction-8.C: New test.
      	* testsuite/libgomp.c++/task-reduction-9.C: New test.
      	* testsuite/libgomp.c/teams-1.c: New test.
      	* testsuite/libgomp.c/teams-2.c: New test.
      	* testsuite/libgomp.c/thread-limit-4.c: New test.
      	* testsuite/libgomp.c/thread-limit-5.c: New test.
      	* testsuite/libgomp.fortran/display-affinity-1.f90: New test.
      
      From-SVN: r265930
      Jakub Jelinek committed
  9. 26 Mar, 2018 1 commit
    • Fix switch conversion in offloading functions · 46dbeb40
      2018-03-26  Tom de Vries  <tom@codesourcery.com>
      
      	PR tree-optimization/85063
      	* omp-general.c (offloading_function_p): New function.  Factor out
      	of ...
      	* omp-offload.c (pass_omp_target_link::gate): ... here.
      	* omp-general.h (offloading_function_p): Declare.
      	* tree-switch-conversion.c (build_one_array): Mark CSWTCH.x variable
      	with attribute omp declare target for offloading functions.
      
      	* testsuite/libgomp.c/switch-conversion-2.c: New test.
      	* testsuite/libgomp.c/switch-conversion.c: New test.
      	* testsuite/libgomp.oacc-c-c++-common/switch-conversion-2.c: New test.
      	* testsuite/libgomp.oacc-c-c++-common/switch-conversion.c: New test.
      
      From-SVN: r258852
      Tom de Vries committed
  10. 03 Jan, 2018 3 commits
    • Update copyright years. · 85ec4feb
      From-SVN: r256169
      Jakub Jelinek committed
    • poly_int: current_vector_size and TARGET_AUTOVECTORIZE_VECTOR_SIZES · 86e36728
      This patch changes the type of current_vector_size to poly_uint64.
      It also changes TARGET_AUTOVECTORIZE_VECTOR_SIZES so that it fills
      in a vector of possible sizes (as poly_uint64s) instead of returning
      a bitmask.  The documentation claimed that the hook didn't need to
      include the default vector size (returned by preferred_simd_mode),
      but that wasn't consistent with the omp-low.c usage.
      
      2018-01-03  Richard Sandiford  <richard.sandiford@linaro.org>
      	    Alan Hayward  <alan.hayward@arm.com>
      	    David Sherwood  <david.sherwood@arm.com>
      
      gcc/
      	* target.h (vector_sizes, auto_vector_sizes): New typedefs.
      	* target.def (autovectorize_vector_sizes): Return the vector sizes
      	by pointer, using vector_sizes rather than a bitmask.
      	* targhooks.h (default_autovectorize_vector_sizes): Update accordingly.
      	* targhooks.c (default_autovectorize_vector_sizes): Likewise.
      	* config/aarch64/aarch64.c (aarch64_autovectorize_vector_sizes):
      	Likewise.
      	* config/arc/arc.c (arc_autovectorize_vector_sizes): Likewise.
      	* config/arm/arm.c (arm_autovectorize_vector_sizes): Likewise.
      	* config/i386/i386.c (ix86_autovectorize_vector_sizes): Likewise.
      	* config/mips/mips.c (mips_autovectorize_vector_sizes): Likewise.
      	* omp-general.c (omp_max_vf): Likewise.
      	* omp-low.c (omp_clause_aligned_alignment): Likewise.
      	* optabs-query.c (can_vec_mask_load_store_p): Likewise.
      	* tree-vect-loop.c (vect_analyze_loop): Likewise.
      	* tree-vect-slp.c (vect_slp_bb): Likewise.
      	* doc/tm.texi: Regenerate.
      	* tree-vectorizer.h (current_vector_size): Change from an unsigned int
      	to a poly_uint64.
      	* tree-vect-stmts.c (get_vectype_for_scalar_type_and_size): Take
      	the vector size as a poly_uint64 rather than an unsigned int.
      	(current_vector_size): Change from an unsigned int to a poly_uint64.
      	(get_vectype_for_scalar_type): Update accordingly.
      	* tree.h (build_truth_vector_type): Take the size and number of
      	units as a poly_uint64 rather than an unsigned int.
      	(build_vector_type): Add a temporary overload that takes
      	the number of units as a poly_uint64 rather than an unsigned int.
      	* tree.c (make_vector_type): Likewise.
      	(build_truth_vector_type): Take the number of units as a poly_uint64
      	rather than an unsigned int.
      
      Co-Authored-By: Alan Hayward <alan.hayward@arm.com>
      Co-Authored-By: David Sherwood <david.sherwood@arm.com>
      
      From-SVN: r256131
      Richard Sandiford committed
    • poly_int: omp_max_vf · 9d2f08ab
      This patch makes omp_max_vf return a polynomial vectorization factor.
      We then need to be able to stash a polynomial value in
      OMP_CLAUSE_SAFELEN_EXPR too:
      
         /* If max_vf is non-zero, then we can use only a vectorization factor
            up to the max_vf we chose.  So stick it into the safelen clause.  */
      
      For now the cfgloop safelen is still constant though.
      
      2018-01-03  Richard Sandiford  <richard.sandiford@linaro.org>
      	    Alan Hayward  <alan.hayward@arm.com>
      	    David Sherwood  <david.sherwood@arm.com>
      
      gcc/
      	* omp-general.h (omp_max_vf): Return a poly_uint64 instead of an int.
      	* omp-general.c (omp_max_vf): Likewise.
      	* omp-expand.c (omp_adjust_chunk_size): Update call to omp_max_vf.
      	(expand_omp_simd): Handle polynomial safelen.
      	* omp-low.c (omplow_simd_context): Add a default constructor.
      	(omplow_simd_context::max_vf): Change from int to poly_uint64.
      	(lower_rec_simd_input_clauses): Update accordingly.
      	(lower_rec_input_clauses): Likewise.
      
      Co-Authored-By: Alan Hayward <alan.hayward@arm.com>
      Co-Authored-By: David Sherwood <david.sherwood@arm.com>
      
      From-SVN: r256129
      Richard Sandiford committed
  11. 28 Nov, 2017 1 commit
    • Remove Cilk Plus support. · 5e9d6aa4
      	* Makefile.def (target_modules): Remove libcilkrts.
      	* Makefile.in: Ditto.
      	* configure: Ditto.
      	* configure.ac: Ditto.
      
      contrib/
      	* contrib/gcc_update: Ditto.
      
      gcc/
      	* Makefile.in (cilkplus.def, cilk-builtins.def, c-family/cilk.o, 
      	c-family/c-cilkplus.o, c-family/array-notation-common.o,
      	cilk-common.o, cilk.h, cilk-common.c): Remove.
      	* builtin-types.def
      	(BT_FN_INT_PTR_PTR_PTR_FTYPE_BT_INT_BT_PTR_BT_PTR_BT_PTR): Remove.
      	* builtins.c (is_builtin_name): Remove cilkplus condition.
      	(BUILT_IN_CILK_DETACH, BUILT_IN_CILK_POP_FRAME): Remove.
      	* builtins.def (DEF_CILK_BUILTIN_STUB, DEF_CILKPLUS_BUILTIN,
      	cilk-builtins.def, cilkplus.def): Remove.
      	* cif-code.def (CILK_SPAWN): Remove.
      	* cilk-builtins.def: Delete.
      	* cilk-common.c: Ditto.
      	* cilk.h: Ditto.
      	* cilkplus.def: Ditto.
      	* config/darwin.h (fcilkplus): Delete.
      	* cppbuiltin.c: Ditto.
      	* doc/extend.texi: Remove cilkplus doc.
      	* doc/generic.texi: Ditto.
      	* doc/invoke.texi: Ditto.
      	* doc/passes.texi: Ditto.
      	* gcc.c (fcilkplus): Remove.
      	* gengtype.c (cilk.h): Remove.
      	* gimple-pretty-print.c (dump_gimple_omp_for): Remove cilkplus support.
      	* gimple.h (GF_OMP_FOR_KIND_CILKFOR, GF_OMP_FOR_KIND_CILKSIMD): Remove.
      	* gimplify.c (gimplify_return_expr, maybe_fold_stmt,
      	gimplify_call_expr, is_gimple_stmt, gimplify_modify_expr,
      	gimplify_scan_omp_clauses, gimplify_adjust_omp_clauses,
      	gimplify_omp_for, gimplify_expr): Remove cilkplus conditions.
      	* ipa-fnsummary.c (ipa_dump_fn_summary, compute_fn_summary,
      	inline_read_section): Ditto.
      	* ipa-inline-analysis.c (cilk.h): Remove.
      	* ira.c (ira_setup_eliminable_regset): Remove cilkplus support.
      	* lto-wrapper.c (merge_and_complain, append_compiler_options,
      	append_linker_options): Remove condition for fcilkplus.
      	* lto/lto-lang.c (cilk.h): Remove.
      	(lto_init): Remove condition for fcilkplus.
      	* omp-expand.c (expand_cilk_for_call): Delete.
      	(expand_omp_taskreg, expand_omp_for_static_chunk,
      	expand_omp_for): Remove cilkplus
      	conditions.
      	(expand_cilk_for): Delete.
      	* omp-general.c (omp_extract_for_data): Remove cilkplus support.
      	* omp-low.c (scan_sharing_clauses, create_omp_child_function,
      	execute_lower_omp, diagnose_sb_0): Ditto.
      	* omp-simd-clone.c (simd_clone_clauses_extract): Ditto.
      	* tree-core.h (OMP_CLAUSE__CILK_FOR_COUNT_): Delete.
      	* tree-nested.c: Ditto.
      	* tree-pretty-print.c (dump_omp_clause): Remove cilkplus support.
      	(dump_generic_node): Ditto.
      	* tree.c (OMP_CLAUSE__CILK_FOR_COUNT_): Delete.
      	* tree.def (cilk_simd, cilk_for, cilk_spawn_stmt,
      	cilk_sync_stmt): Delete.
      	* tree.h (CILK_SPAWN_FN, EXPR_CILK_SPAWN): Delete.
      
      gcc/c-family/
      	* array-notation-common.c: Delete.
      	* c-cilkplus.c: Ditto.
      	* c-common.c (_Cilk_spawn, _Cilk_sync, _Cilk_for): Remove.
      	* c-common.def (ARRAY_NOTATION_REF): Remove.
      	* c-common.h (RID_CILK_SPAWN, build_array_notation_expr,
      	build_array_notation_ref, C_ORT_CILK, c_check_cilk_loop,
      	c_validate_cilk_plus_loop, cilkplus_an_parts,
      	cilk_ignorable_spawn_rhs_op,
      	cilk_recognize_spawn): Remove.
      	* c-gimplify.c (CILK_SPAWN_STMT): Remove.
      	* c-omp.c: Remove CILK_SIMD check.
      	* c-pragma.c: Ditto.
      	* c-pragma.h: Remove CILK related pragmas.
      	* c-pretty-print.c (c_pretty_printer::postfix_expression): Remove
      	ARRAY_NOTATION_REF condition.
      	(c_pretty_printer::expression): Ditto.
      	* c.opt (fcilkplus): Remove.
      	* cilk.c: Delete.
      
      gcc/c/
      	* Make-lang.in (c/c-array-notation.o): Remove.
      	* c-array-notation.c: Delete.
      	* c-decl.c: Remove cilkplus condition.
      	* c-parser.c (c_parser_cilk_simd, c_parser_cilk_for,
      	c_parser_cilk_verify_simd, c_parser_array_notation,
      	c_parser_cilk_clause_vectorlength, c_parser_cilk_grainsize,
      	c_parser_cilk_simd_fn_vector_attrs,
      	c_finish_cilk_simd_fn_tokens): Delete.
      	(c_parser_declaration_or_fndef): Remove cilkplus condition.
      	(c_parser_direct_declarator_inner): Ditto.
      	(CILK_SIMD_FN_CLAUSE_MASK): Delete.
      	(c_parser_attributes, c_parser_compound_statement,
      	c_parser_statement_after_labels, c_parser_if_statement,
      	c_parser_switch_statement, c_parser_while_statement,
      	c_parser_do_statement, c_parser_for_statement,
      	c_parser_unary_expression, c_parser_postfix_expression,
      	c_parser_postfix_expression_after_primary,
      	c_parser_pragma, c_parser_omp_clause_name, c_parser_omp_all_clauses,
      	c_parser_omp_for_loop,
      	c_finish_omp_declare_simd): Remove cilkplus support.
      	* c-typeck.c (build_array_ref, build_function_call_vec,
      	convert_arguments, lvalue_p, build_compound_expr, c_finish_return,
      	c_finish_if_stmt, c_finish_loop,
      	build_binary_op): Remove cilkplus support.
      	
      gcc/cp/
      	* Make-lang.in (cp/cp-array-notation.o, cp/cp-cilkplus.o): Delete.
      	* call.c (convert_for_arg_passing, build_cxx_call): Remove cilkplus.
      	* constexpr.c (potential_constant_expression_1): Ditto.
      	* cp-array-notation.c: Delete.
      	* cp-cilkplus.c: Ditto.
      	* cp-cilkplus.h: Ditto.
      	* cp-gimplify.c (cp_gimplify_expr, cp_fold_r, cp_genericize): Remove
      	cilkplus condition.
      	* cp-objcp-common.c (ARRAY_NOTATION_REF): Delete.
      	* cp-tree.h (cilkplus_an_triplet_types_ok_p): Delete.
      	* decl.c (grokfndecl, finish_function): Remove cilkplus condition.
      	* error.c (dump_decl, dump_expr): Remove ARRAY_NOTATION_REF condition.
      	* lambda.c (cp-cilkplus.h): Remove.
      	* parser.c (cp_parser_cilk_simd, cp_parser_cilk_for,
      	cp_parser_cilk_simd_vectorlength): Delete.
      	(cp_debug_parser, cp_parser_ctor_initializer_opt_and_function_body,
      	cp_parser_postfix_expression, cp_parser_postfix_open_square_expression,
      	cp_parser_statement, cp_parser_jump_statement,
      	cp_parser_direct_declarator,
      	cp_parser_late_return_type_opt, cp_parser_gnu_attribute_list,
      	cp_parser_omp_clause_name, cp_parser_omp_clause_aligned,
      	cp_parser_omp_clause_linear, cp_parser_omp_all_clauses,
      	cp_parser_omp_flush, cp_parser_omp_for_cond, cp_parser_omp_for_incr,
      	cp_parser_omp_for_loop_init, cp_parser_omp_for_loop,
      	cp_parser_omp_declare_simd): Remove cilkplus support.
      	(CILK_SIMD_FN_CLAUSE_MASK, cp_parser_late_parsing_cilk_simd_fn_info,
      	cp_parser_cilk_grainsize): Remove.
      	(cp_parser_pragma, c_parse_file): Remove cilkplus support.
      	(cp_parser_cilk_simd_vectorlength, cp_parser_cilk_simd_linear,
      	cp_parser_cilk_simd_clause_name, cp_parser_cilk_simd_all_clauses,
      	cp_parser_cilk_simd, cp_parser_cilk_for): Remove.
      	* parser.h (IN_CILK_SIMD_FOR, IN_CILK_SPAWN): Remove.
      	* pt.c (tsubst_attribute, tsubst_expr, tsubst_copy_and_build): Remove
      	cilkplus support.
      	* semantics.c (finish_goto_stmt, begin_while_stmt, finish_do_body,
      	finish_init_stmt, finish_switch_cond, simplify_aggr_init_expr,
      	finish_omp_clauses, finish_omp_clauses,
      	finish_omp_for): Remove cilkplus support.
      	* tree.c (lvalue_kind): Remove ARRAY_NOTATION_REF conditon.
      	* typeck.c (cp_build_array_ref, cp_build_compound_expr,
      	check_return_expr): Remove cilkplus support.
      
      gcc/testsuite/
      	* c-c++-common/attr-simd-3.c: Delete.
      	* c-c++-common/cilk-plus/AN/an-if.c: Delete.
      	* c-c++-common/cilk-plus/AN/array_test1.c: Delete.
      	* c-c++-common/cilk-plus/AN/array_test2.c: Delete.
      	* c-c++-common/cilk-plus/AN/array_test_ND.c: Delete.
      	* c-c++-common/cilk-plus/AN/builtin_fn_custom.c: Delete.
      	* c-c++-common/cilk-plus/AN/builtin_fn_mutating.c: Delete.
      	* c-c++-common/cilk-plus/AN/builtin_func_double.c: Delete.
      	* c-c++-common/cilk-plus/AN/builtin_func_double2.c: Delete.
      	* c-c++-common/cilk-plus/AN/comma_exp.c: Delete.
      	* c-c++-common/cilk-plus/AN/conditional.c: Delete.
      	* c-c++-common/cilk-plus/AN/decl-ptr-colon.c: Delete.
      	* c-c++-common/cilk-plus/AN/dimensionless-arrays.c: Delete.
      	* c-c++-common/cilk-plus/AN/exec-once.c: Delete.
      	* c-c++-common/cilk-plus/AN/exec-once2.c: Delete.
      	* c-c++-common/cilk-plus/AN/fn_ptr-2.c: Delete.
      	* c-c++-common/cilk-plus/AN/fn_ptr.c: Delete.
      	* c-c++-common/cilk-plus/AN/fp_triplet_values.c: Delete.
      	* c-c++-common/cilk-plus/AN/gather-scatter-errors.c: Delete.
      	* c-c++-common/cilk-plus/AN/gather_scatter.c: Delete.
      	* c-c++-common/cilk-plus/AN/if_test.c: Delete.
      	* c-c++-common/cilk-plus/AN/if_test_errors.c: Delete.
      	* c-c++-common/cilk-plus/AN/misc.c: Delete.
      	* c-c++-common/cilk-plus/AN/n-ptr-test.c: Delete.
      	* c-c++-common/cilk-plus/AN/parser_errors.c: Delete.
      	* c-c++-common/cilk-plus/AN/parser_errors2.c: Delete.
      	* c-c++-common/cilk-plus/AN/parser_errors3.c: Delete.
      	* c-c++-common/cilk-plus/AN/parser_errors4.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr57457-2.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr57457.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr57490.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr57541-2.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr57541.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr57577.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr58942.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr61191.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr61455-2.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr61455.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr61962.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr61963.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr62008.c: Delete.
      	* c-c++-common/cilk-plus/AN/pr63884.c: Delete.
      	* c-c++-common/cilk-plus/AN/rank_mismatch.c: Delete.
      	* c-c++-common/cilk-plus/AN/rank_mismatch2.c: Delete.
      	* c-c++-common/cilk-plus/AN/rank_mismatch3.c: Delete.
      	* c-c++-common/cilk-plus/AN/sec_implicit.c: Delete.
      	* c-c++-common/cilk-plus/AN/sec_implicit2.c: Delete.
      	* c-c++-common/cilk-plus/AN/sec_implicit_ex.c: Delete.
      	* c-c++-common/cilk-plus/AN/sec_reduce_ind_same_value.c: Delete.
      	* c-c++-common/cilk-plus/AN/sec_reduce_max_min_ind.c: Delete.
      	* c-c++-common/cilk-plus/AN/sec_reduce_return.c: Delete.
      	* c-c++-common/cilk-plus/AN/side-effects-1.c: Delete.
      	* c-c++-common/cilk-plus/AN/test_builtin_return.c: Delete.
      	* c-c++-common/cilk-plus/AN/test_sec_limits.c: Delete.
      	* c-c++-common/cilk-plus/AN/tst_lngth.c: Delete.
      	* c-c++-common/cilk-plus/AN/vla.c: Delete.
      	* c-c++-common/cilk-plus/CK/Wparentheses-1.c: Delete.
      	* c-c++-common/cilk-plus/CK/cilk-for-2.c: Delete.
      	* c-c++-common/cilk-plus/CK/cilk-for-3.c: Delete.
      	* c-c++-common/cilk-plus/CK/cilk-fors.c: Delete.
      	* c-c++-common/cilk-plus/CK/cilk_for_errors.c: Delete.
      	* c-c++-common/cilk-plus/CK/cilk_for_grain.c: Delete.
      	* c-c++-common/cilk-plus/CK/cilk_for_grain_errors.c: Delete.
      	* c-c++-common/cilk-plus/CK/cilk_for_ptr_iter.c: Delete.
      	* c-c++-common/cilk-plus/CK/compound_cilk_spawn.c: Delete.
      	* c-c++-common/cilk-plus/CK/concec_cilk_spawn.c: Delete.
      	* c-c++-common/cilk-plus/CK/errors.c: Delete.
      	* c-c++-common/cilk-plus/CK/fib.c: Delete.
      	* c-c++-common/cilk-plus/CK/fib_init_expr_xy.c: Delete.
      	* c-c++-common/cilk-plus/CK/fib_no_return.c: Delete.
      	* c-c++-common/cilk-plus/CK/fib_no_sync.c: Delete.
      	* c-c++-common/cilk-plus/CK/invalid_spawns.c: Delete.
      	* c-c++-common/cilk-plus/CK/invalid_sync.c: Delete.c
      	* c-c++-common/cilk-plus/CK/nested_cilk_for.c: Delete.
      	* c-c++-common/cilk-plus/CK/no_args_error.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr59631.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr60197-2.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr60197.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr60469.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr60586.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr63307.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr69826-1.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr69826-2.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr79428-4.c: Delete.
      	* c-c++-common/cilk-plus/CK/pr79428-7.c: Delete.
      	* c-c++-common/cilk-plus/CK/spawn_in_return.c: Delete.
      	* c-c++-common/cilk-plus/CK/spawnee_inline.c: Delete.
      	* c-c++-common/cilk-plus/CK/spawner_inline.c: Delete.
      	* c-c++-common/cilk-plus/CK/spawning_arg.c: Delete.
      	* c-c++-common/cilk-plus/CK/steal_check.c: Delete.
      	* c-c++-common/cilk-plus/CK/sync_wo_spawn.c: Delete.
      	* c-c++-common/cilk-plus/CK/test__cilk.c: Delete.
      	* c-c++-common/cilk-plus/CK/varargs_test.c: Delete.
      	* c-c++-common/cilk-plus/PS/Wparentheses-1.c: Delete.
      	* c-c++-common/cilk-plus/PS/body.c: Delete.
      	* c-c++-common/cilk-plus/PS/clauses1.c: Delete.
      	* c-c++-common/cilk-plus/PS/clauses2.c: Delete.
      	* c-c++-common/cilk-plus/PS/clauses3.c: Delete.
      	* c-c++-common/cilk-plus/PS/clauses4.c: Delete.
      	* c-c++-common/cilk-plus/PS/for1.c: Delete.
      	* c-c++-common/cilk-plus/PS/for2.c: Delete.
      	* c-c++-common/cilk-plus/PS/for3.c: Delete.
      	* c-c++-common/cilk-plus/PS/pr69363.c: Delete.
      	* c-c++-common/cilk-plus/PS/reduction-1.c: Delete.
      	* c-c++-common/cilk-plus/PS/reduction-2.c: Delete.
      	* c-c++-common/cilk-plus/PS/reduction-3.c: Delete.
      	* c-c++-common/cilk-plus/PS/run-1.c: Delete.
      	* c-c++-common/cilk-plus/PS/safelen.c: Delete.
      	* c-c++-common/cilk-plus/PS/vectorlength-2.c: Delete.
      	* c-c++-common/cilk-plus/PS/vectorlength-3.c: Delete.
      	* c-c++-common/cilk-plus/PS/vectorlength.c: Delete.
      	* c-c++-common/cilk-plus/SE/ef_error.c: Delete.
      	* c-c++-common/cilk-plus/SE/ef_error2.c: Delete.
      	* c-c++-common/cilk-plus/SE/ef_error3.c: Delete.
      	* c-c++-common/cilk-plus/SE/ef_test.c: Delete.
      	* c-c++-common/cilk-plus/SE/ef_test2.c: Delete.
      	* c-c++-common/cilk-plus/SE/vlength_errors.c: Delete.
      	* g++.dg/cilk-plus/AN/array_function.c: Delete.
      	* g++.dg/cilk-plus/AN/array_test1_tplt.c: Delete.
      	* g++.dg/cilk-plus/AN/array_test2_tplt.c: Delete.
      	* g++.dg/cilk-plus/AN/array_test_ND_tplt.c: Delete.
      	* g++.dg/cilk-plus/AN/braced_list.c: Delete.
      	* g++.dg/cilk-plus/AN/builtin_fn_custom_tplt.c: Delete.
      	* g++.dg/cilk-plus/AN/builtin_fn_mutating_tplt.c: Delete.
      	* g++.dg/cilk-plus/AN/fp_triplet_values_tplt.c: Delete.
      	* g++.dg/cilk-plus/AN/postincr_test.c: Delete.
      	* g++.dg/cilk-plus/AN/preincr_test.c: Delete.
      	* g++.dg/cilk-plus/CK/catch_exc.c: Delete.
      	* g++.dg/cilk-plus/CK/cf3.c: Delete.
      	* g++.dg/cilk-plus/CK/cilk-for-tplt.c: Delete.
      	* g++.dg/cilk-plus/CK/const_spawn.c: Delete.
      	* g++.dg/cilk-plus/CK/fib-opr-overload.c: Delete.
      	* g++.dg/cilk-plus/CK/fib-tplt.c: Delete.
      	* g++.dg/cilk-plus/CK/for1.c: Delete.
      	* g++.dg/cilk-plus/CK/lambda_spawns.c: Delete.
      	* g++.dg/cilk-plus/CK/lambda_spawns_tplt.c: Delete.
      	* g++.dg/cilk-plus/CK/pr60586.c: Delete.
      	* g++.dg/cilk-plus/CK/pr66326.c: Delete.
      	* g++.dg/cilk-plus/CK/pr68001.c: Delete.
      	* g++.dg/cilk-plus/CK/pr68997.c: Delete.
      	* g++.dg/cilk-plus/CK/pr69024.c: Delete.
      	* g++.dg/cilk-plus/CK/pr69048.c: Delete.
      	* g++.dg/cilk-plus/CK/pr69267.c: Delete.
      	* g++.dg/cilk-plus/CK/pr80038.c: Delete.
      	* g++.dg/cilk-plus/CK/stl_iter.c: Delete.
      	* g++.dg/cilk-plus/CK/stl_rev_iter.c: Delete.
      	* g++.dg/cilk-plus/CK/stl_test.c: Delete.
      	* g++.dg/cilk-plus/cilk-plus.exp
      	* g++.dg/cilk-plus/ef_test.C: Delete.
      	* g++.dg/cilk-plus/for.C: Delete.
      	* g++.dg/cilk-plus/for2.C: Delete.
      	* g++.dg/cilk-plus/for3.C: Delete.
      	* g++.dg/cilk-plus/for4.C: Delete.
      	* g++.dg/cilk-plus/pr60967.C: Delete.
      	* g++.dg/cilk-plus/pr69028.C: Delete.
      	* g++.dg/cilk-plus/pr70565.C: Delete.
      	* g++.dg/pr57662.C: Delete.
      	* gcc.dg/cilk-plus/cilk-plus.exp
      	* gcc.dg/cilk-plus/for1.c: Delete.
      	* gcc.dg/cilk-plus/for2.c: Delete.
      	* gcc.dg/cilk-plus/jump-openmp.c: Delete.
      	* gcc.dg/cilk-plus/jump.c: Delete.
      	* gcc.dg/cilk-plus/pr69798-1.c: Delete.
      	* gcc.dg/cilk-plus/pr69798-2.c: Delete.
      	* gcc.dg/cilk-plus/pr78306.c: Delete.
      	* gcc.dg/cilk-plus/pr79116.c: Delete.
      	* gcc.dg/graphite/id-28.c: Delete.
      	* lib/cilk-plus-dg.exp: Delete.
      	* lib/target-supports.exp (cilkplus_runtime): Delete.
      
      Co-Authored-By: Sebastian Peryt <sebastian.peryt@intel.com>
      
      From-SVN: r255195
      Julia Koval committed
  12. 08 Aug, 2017 1 commit
    • trans.c: Include header files. · 314e6352
      .
      2017-08-08  Martin Liska  <mliska@suse.cz>
      
      	* gcc-interface/trans.c: Include header files.
      2017-08-08  Martin Liska  <mliska@suse.cz>
      
      	* objc-gnu-runtime-abi-01.c: Include header files.
      	* objc-next-runtime-abi-01.c: Likewise.
      	* objc-next-runtime-abi-02.c: Likewise.
      2017-08-08  Martin Liska  <mliska@suse.cz>
      
      	* asan.c: Include header files.
      	* attribs.c (build_decl_attribute_variant): New function moved
      	from tree.[ch].
      	(build_type_attribute_qual_variant): Likewise.
      	(cmp_attrib_identifiers): Likewise.
      	(simple_cst_list_equal): Likewise.
      	(omp_declare_simd_clauses_equal): Likewise.
      	(attribute_value_equal): Likewise.
      	(comp_type_attributes): Likewise.
      	(build_type_attribute_variant): Likewise.
      	(lookup_ident_attribute): Likewise.
      	(remove_attribute): Likewise.
      	(merge_attributes): Likewise.
      	(merge_type_attributes): Likewise.
      	(merge_decl_attributes): Likewise.
      	(merge_dllimport_decl_attributes): Likewise.
      	(handle_dll_attribute): Likewise.
      	(attribute_list_equal): Likewise.
      	(attribute_list_contained): Likewise.
      	* attribs.h (lookup_attribute): New function moved from tree.[ch].
      	(lookup_attribute_by_prefix): Likewise.
      	* bb-reorder.c: Include header files.
      	* builtins.c: Likewise.
      	* calls.c: Likewise.
      	* cfgexpand.c: Likewise.
      	* cgraph.c: Likewise.
      	* cgraphunit.c: Likewise.
      	* convert.c: Likewise.
      	* dwarf2out.c: Likewise.
      	* final.c: Likewise.
      	* fold-const.c: Likewise.
      	* function.c: Likewise.
      	* gimple-expr.c: Likewise.
      	* gimple-fold.c: Likewise.
      	* gimple-pretty-print.c: Likewise.
      	* gimple.c: Likewise.
      	* gimplify.c: Likewise.
      	* hsa-common.c: Likewise.
      	* hsa-gen.c: Likewise.
      	* internal-fn.c: Likewise.
      	* ipa-chkp.c: Likewise.
      	* ipa-cp.c: Likewise.
      	* ipa-devirt.c: Likewise.
      	* ipa-fnsummary.c: Likewise.
      	* ipa-inline.c: Likewise.
      	* ipa-visibility.c: Likewise.
      	* ipa.c: Likewise.
      	* lto-cgraph.c: Likewise.
      	* omp-expand.c: Likewise.
      	* omp-general.c: Likewise.
      	* omp-low.c: Likewise.
      	* omp-offload.c: Likewise.
      	* omp-simd-clone.c: Likewise.
      	* opts-global.c: Likewise.
      	* passes.c: Likewise.
      	* predict.c: Likewise.
      	* sancov.c: Likewise.
      	* sanopt.c: Likewise.
      	* symtab.c: Likewise.
      	* toplev.c: Likewise.
      	* trans-mem.c: Likewise.
      	* tree-chkp.c: Likewise.
      	* tree-eh.c: Likewise.
      	* tree-into-ssa.c: Likewise.
      	* tree-object-size.c: Likewise.
      	* tree-parloops.c: Likewise.
      	* tree-profile.c: Likewise.
      	* tree-ssa-ccp.c: Likewise.
      	* tree-ssa-live.c: Likewise.
      	* tree-ssa-loop.c: Likewise.
      	* tree-ssa-sccvn.c: Likewise.
      	* tree-ssa-structalias.c: Likewise.
      	* tree-ssa.c: Likewise.
      	* tree-streamer-in.c: Likewise.
      	* tree-vectorizer.c: Likewise.
      	* tree-vrp.c: Likewise.
      	* tsan.c: Likewise.
      	* ubsan.c: Likewise.
      	* varasm.c: Likewise.
      	* varpool.c: Likewise.
      	* tree.c: Remove functions moved to attribs.[ch].
      	* tree.h: Likewise.
      	* config/aarch64/aarch64.c: Add attrs.h header file.
      	* config/alpha/alpha.c: Likewise.
      	* config/arc/arc.c: Likewise.
      	* config/arm/arm.c: Likewise.
      	* config/avr/avr.c: Likewise.
      	* config/bfin/bfin.c: Likewise.
      	* config/c6x/c6x.c: Likewise.
      	* config/cr16/cr16.c: Likewise.
      	* config/cris/cris.c: Likewise.
      	* config/darwin.c: Likewise.
      	* config/epiphany/epiphany.c: Likewise.
      	* config/fr30/fr30.c: Likewise.
      	* config/frv/frv.c: Likewise.
      	* config/ft32/ft32.c: Likewise.
      	* config/h8300/h8300.c: Likewise.
      	* config/i386/winnt.c: Likewise.
      	* config/ia64/ia64.c: Likewise.
      	* config/iq2000/iq2000.c: Likewise.
      	* config/lm32/lm32.c: Likewise.
      	* config/m32c/m32c.c: Likewise.
      	* config/m32r/m32r.c: Likewise.
      	* config/m68k/m68k.c: Likewise.
      	* config/mcore/mcore.c: Likewise.
      	* config/microblaze/microblaze.c: Likewise.
      	* config/mips/mips.c: Likewise.
      	* config/mmix/mmix.c: Likewise.
      	* config/mn10300/mn10300.c: Likewise.
      	* config/moxie/moxie.c: Likewise.
      	* config/msp430/msp430.c: Likewise.
      	* config/nds32/nds32-isr.c: Likewise.
      	* config/nds32/nds32.c: Likewise.
      	* config/nios2/nios2.c: Likewise.
      	* config/nvptx/nvptx.c: Likewise.
      	* config/pa/pa.c: Likewise.
      	* config/pdp11/pdp11.c: Likewise.
      	* config/powerpcspe/powerpcspe.c: Likewise.
      	* config/riscv/riscv.c: Likewise.
      	* config/rl78/rl78.c: Likewise.
      	* config/rx/rx.c: Likewise.
      	* config/s390/s390.c: Likewise.
      	* config/sh/sh.c: Likewise.
      	* config/sol2.c: Likewise.
      	* config/sparc/sparc.c: Likewise.
      	* config/spu/spu.c: Likewise.
      	* config/stormy16/stormy16.c: Likewise.
      	* config/tilegx/tilegx.c: Likewise.
      	* config/tilepro/tilepro.c: Likewise.
      	* config/v850/v850.c: Likewise.
      	* config/vax/vax.c: Likewise.
      	* config/visium/visium.c: Likewise.
      	* config/xtensa/xtensa.c: Likewise.
      2017-08-08  Martin Liska  <mliska@suse.cz>
      
      	* call.c: Include header files.
      	* cp-gimplify.c: Likewise.
      	* cp-ubsan.c: Likewise.
      	* cvt.c: Likewise.
      	* init.c: Likewise.
      	* search.c: Likewise.
      	* semantics.c: Likewise.
      	* typeck.c: Likewise.
      2017-08-08  Martin Liska  <mliska@suse.cz>
      
      	* lto-lang.c: Include header files.
      	* lto-symtab.c: Likewise.
      2017-08-08  Martin Liska  <mliska@suse.cz>
      
      	* c-convert.c: Include header files.
      	* c-typeck.c: Likewise.
      2017-08-08  Martin Liska  <mliska@suse.cz>
      
      	* c-ada-spec.c: Include header files.
      	* c-ubsan.c: Likewise.
      	* c-warn.c: Likewise.
      2017-08-08  Martin Liska  <mliska@suse.cz>
      
      	* trans-types.c: Include header files.
      
      From-SVN: r250946
      Martin Liska committed
  13. 01 Aug, 2017 1 commit
    • Remove flag_tree_vectorize · 26d476cd
      gcc/
      
      	* common.opt (ftree-vectorize): No longer set flag_tree_vectorize.
      	(ftree-loop-vectorize): Set as EnabledBy ftree-vectorize.
      	(ftree-slp-vectorize): Likewise.
      	* omp-expand (expand_omp_simd): Remove flag_tree_vectorize, as it
      	can no longer be set independent of flag_tree_loop_vectorize.
      	* omp-general.c (emp_max_vf): Likewise.
      	* opts.c (enable_fdo_optimizations): Remove references to
      	flag_tree_vectorize, these are now implicit.
      	(common_handle_option): Remove handling for OPT_ftree_vectorize,
      	and leave it for the options machinery.
      
      From-SVN: r250774
      James Greenhalgh committed
  14. 12 May, 2017 1 commit
    • Use "oacc kernels" attribute for OpenACC kernels · 25651634
      	gcc/
      	* omp-expand.c (expand_omp_target) <GF_OMP_TARGET_KIND_OACC_KERNELS>:
      	Set "oacc kernels" attribute.
      	* omp-general.c (oacc_set_fn_attrib): Remove is_kernel formal
      	parameter.  Adjust all users.
      	(oacc_fn_attrib_kernels_p): Remove function.
      	* omp-offload.c (execute_oacc_device_lower): Look for "oacc
      	kernels" attribute instead of calling oacc_fn_attrib_kernels_p.
      	* tree-ssa-loop.c (gate_oacc_kernels): Likewise.
      	* tree-parloops.c (create_parallel_loop): If oacc_kernels_p,
      	assert "oacc kernels" attribute is set.
      	gcc/testsuite/
      	* c-c++-common/goacc/classify-kernels-unparallelized.c: Adjust.
      	* c-c++-common/goacc/classify-kernels.c: Likewise.
      	* c-c++-common/goacc/classify-parallel.c: Likewise.
      	* c-c++-common/goacc/classify-routine.c: Likewise.
      	* gfortran.dg/goacc/classify-kernels-unparallelized.f95: Likewise.
      	* gfortran.dg/goacc/classify-kernels.f95: Likewise.
      	* gfortran.dg/goacc/classify-parallel.f95: Likewise.
      	* gfortran.dg/goacc/classify-routine.f95: Likewise.
      
      From-SVN: r247955
      Thomas Schwinge committed
  15. 09 Feb, 2017 1 commit
    • gimplify.c (gimplify_scan_omp_clauses): No special handling for OMP_CLAUSE_TILE. · 02889d23
      2017-02-09  Nathan Sidwell  <nathan@codesourcery.com>
      	    Cesar Philippidis  <cesar@codesourcery.com>
      	    Joseph Myers  <joseph@codesourcery.com>
      	    Chung-Lin Tang  <cltang@codesourcery.com>
      
      	gcc/
      	* gimplify.c (gimplify_scan_omp_clauses): No special handling for
      	OMP_CLAUSE_TILE.
      	(gimplify_adjust_omp_clauses): Don't delete TILE.
      	(gimplify_omp_for): Deal with TILE.
      	* internal-fn.c (expand_GOACC_TILE): New function.
      	* internal-fn.def (GOACC_DIM_POS): Comment may be overly conservative.
      	(GOACC_TILE): New.
      	* omp-expand.c (struct oacc_collapse): Add tile and outer fields.
      	(expand_oacc_collapse_init): Add LOC paramter.  Initialize tile
      	element fields.
      	(expand_oacc_collapse_vars): Add INNER parm, adjust for tiling,
      	avoid DIV for outermost collapse var.
      	(expand_oacc_for): Insert tile element loop as needed.  Adjust.
      	Remove out of date comments, fix whitespace.
      	* omp-general.c (omp_extract_for_data): Deal with tiling.
      	* omp-general.h (enum oacc_loop_flags): Add OLF_TILE flag,
      	adjust OLF_DIM_BASE value.
      	(struct omp_for_data): Add tiling field.
      	* omp-low.c (scan_sharing_clauses): Allow OMP_CLAUSE_TILE.
      	(lower_oacc_head_mark): Add OLF_TILE as appropriate.  Ensure 2 levels
      	for auto loops.  Remove default auto determining, moved to
      	oacc_loop_fixed_partitions.
      	* omp-offload.c (struct oacc_loop): Change 'ifns' to vector of call
      	stmts, add e_mask field.
      	(oacc_dim_call): New function, abstracted out from oacc_thread_numbers.
      	(oacc_thread_numbers): Use oacc_dim_call.
      	(oacc_xform_tile): New.
      	(new_oacc_loop_raw): Initialize e_mask, adjust for ifns vector.
      	(finish_oacc_loop): Adjust for ifns vector.
      	(oacc_loop_discover_walk): Append loop abstraction sites to list,
      	add case for GOACC_TILE fns.
      	(oacc_loop_xform_loop): Delete.
      	(oacc_loop_process): Iterate over call list directly, and add
      	handling for GOACC_TILE fns.
      	(oacc_loop_fixed_partitions): Determine default auto, deal with TILE,
      	dump partitioning.
      	(oacc_loop_auto_partitions): Add outer_assign parm. Assign all but
      	vector partitioning to outer loops.  Assign 2 partitions to loops
      	when available. Add TILE handling.
      	(oacc_loop_partition): Adjust oacc_loop_auto_partitions call.
      	(execite_oacc_device_lower): Process GOACC_TILE fns, ignore unknown specs.
      	* tree-nested.c (convert_nonlocal_omp_clauses): Allow OMP_CLAUSE_TILE.
      	* tree.c (omp_clause_num_ops): Adjust TILE ops.
      	* tree.h (OMP_CLAUSE_TILE_ITERVAR, OMP_CLAUSE_TILE_COUNT): New.
      
      	gcc/c/
      	* c-parser.c (c_parser_omp_clause_collapse): Disallow tile.
      	(c_parser_oacc_clause_tile): Disallow collapse. Fix parsing and
      	semantic checking.
      	* c-parser.c (c_parser_omp_for_loop): Accept tiling constructs.
      
      	gcc/cp/
      	* parser.c (cp_parser_oacc_clause_tile): Disallow collapse.  Fix
      	parsing.  Parse constant expression. Remove semantic checking.
      	(cp_parser_omp_clause_collapse): Disallow tile.
      	(cp_parser_omp_for_loop): Deal with tile clause.  Don't emit a parse
      	error about missing for after already emitting one.  Use more
      	conventional for idiom for unbounded loop.
      	* pt.c (tsubst_omp_clauses): Handle OMP_CLAUSE_TILE.
      	* semantics.c (finish_omp_clauses): Correct TILE semantic check.
      	(finish_omp_for): Deal with tile clause.
      
      	gcc/fortran/
      	* openmp.c (resolve_omp_clauses): Error on directives
      	containing both tile and collapse clauses.
      	(resolve_oacc_loop_blocks): Represent '*' tile arguments as zero.
      	* trans-openmp.c (gfc_trans_omp_do): Lower tiled loops like
      	collapsed loops.
      
      	gcc/testsuite/
      	* c-c++-common/goacc/combined-directives.c: Remove xfail.
      	* c-c++-common/goacc/loop-auto-1.c: Adjust and add additional case.
      	* c-c++-common/goacc/loop-auto-2.c: New.
      	* c-c++-common/goacc/tile.c: Include stdbool, fix expected errors.
      	* c-c++-common/goacc/tile-2.c: New.
      	* g++.dg/goacc/template.C: Test tile subst.  Adjust erroneous uses.
      	* g++.dg/goacc/tile-1.C: New, check tile subst.
      	* gcc.dg/goacc/loop-processing-1.c: Adjust dg-final pattern.
      	* gfortran.dg/goacc/combined-directives.f90: Remove xfail.
      	* gfortran.dg/goacc/tile-1.f90: New test.
      	* gfortran.dg/goacc/tile-2.f90: New test.
      	* gfortran.dg/goacc/tile-lowering.f95: New test.
      
      	libgomp/
      	* testsuite/libgomp.oacc-c-c++-common/tile-1.c: New.
      	* testsuite/libgomp.oacc-c-c++-common/loop-auto-1.c: Adjust and
      	add additional case.
      	* testsuite/libgomp.oacc-c-c++-common/vprop.c: XFAIL under
      	"openacc_nvidia_accel_selected".
      	* libgomp.oacc-fortran/nested-function-1.f90 (test2):
      	Add num_workers(8) clause.
      
      From-SVN: r245300
      Chung-Lin Tang committed
  16. 01 Jan, 2017 1 commit
  17. 14 Dec, 2016 2 commits
    • Coding style fixes · 01914336
      2016-12-14  Martin Jambor  <mjambor@suse.cz>
      
      	    * omp-offload.c: Fix coding style.
      	    * omp-expand.c: Likewise.
      	    * omp-general.c: Likewise.
      	    * omp-grid.c: Likewise.
      	    * omp-low.c: Fix coding style of parts touched by the
      	      previous splitting patch.
      
      From-SVN: r243674
      Martin Jambor committed
    • Split omp-low into multiple files · 629b3d75
      2016-12-14  Martin Jambor  <mjambor@suse.cz>
      
      	* omp-general.h: New file.
      	* omp-general.c: New file.
      	* omp-expand.h: Likewise.
      	* omp-expand.c: Likewise.
      	* omp-offload.h: Likewise.
      	* omp-offload.c: Likewise.
      	* omp-grid.c: Likewise.
      	* omp-grid.c: Likewise.
      	* omp-low.h: Include omp-general.h and omp-grid.h.  Removed includes
      	of params.h, symbol-summary.h, lto-section-names.h, cilk.h, tree-eh.h,
      	ipa-prop.h, tree-cfgcleanup.h, cfgloop.h, except.h, expr.h, stmt.h,
      	varasm.h, calls.h, explow.h, dojump.h, flags.h, tree-into-ssa.h,
      	tree-cfg.h, cfganal.h, alias.h, emit-rtl.h, optabs.h, expmed.h,
      	alloc-pool.h, cfghooks.h, rtl.h and memmodel.h.
      	(omp_find_combined_for): Declare.
      	(find_omp_clause): Renamed to omp_find_clause and moved to
      	omp-general.h.
      	(free_omp_regions): Renamed to omp_free_regions and moved to
      	omp-expand.h.
      	(replace_oacc_fn_attrib): Renamed to oacc_replace_fn_attrib and moved
      	to omp-general.h.
      	(set_oacc_fn_attrib): Renamed to oacc_set_fn_attrib and moved to
      	omp-general.h.
      	(build_oacc_routine_dims): Renamed to oacc_build_routine_dims and
      	moved to omp-general.h.
      	(get_oacc_fn_attrib): Renamed to oacc_get_fn_attrib and moved to
      	omp-general.h.
      	(oacc_fn_attrib_kernels_p): Moved to omp-general.h.
      	(get_oacc_fn_dim_size): Renamed to oacc_get_fn_dim_size and moved to
      	omp-general.c.
      	(omp_expand_local): Moved to omp-expand.h.
      	(make_gimple_omp_edges): Renamed to omp_make_gimple_edges and moved to
      	omp-expand.h.
      	(omp_finish_file): Moved to omp-offload.h.
      	(default_goacc_validate_dims): Renamed to
      	oacc_default_goacc_validate_dims and moved to omp-offload.h.
      	(offload_funcs, offload_vars): Moved to omp-offload.h.
      	* omp-low.c: Include omp-general.h, omp-offload.h and omp-grid.h.
      	(omp_region): Moved to omp-expand.c.
      	(omp_for_data_loop): Moved to omp-general.h.
      	(omp_for_data): Likewise.
      	(oacc_loop): Moved to omp-offload.c.
      	(oacc_loop_flags): Moved to omp-general.h.
      	(offload_funcs, offload_vars): Moved to omp-offload.c.
      	(root_omp_region): Moved to omp-expand.c.
      	(omp_any_child_fn_dumped): Likewise.
      	(find_omp_clause): Renamed to omp_find_clause and moved to
      	omp-general.c.
      	(is_combined_parallel): Moved to omp-expand.c.
      	(is_reference): Renamed to omp_is_reference and and moved to
      	omp-general.c.
      	(adjust_for_condition): Renamed to omp_adjust_for_condition and moved
      	to omp-general.c.
      	(get_omp_for_step_from_incr): Renamed to omp_get_for_step_from_incr
      	and moved to omp-general.c.
      	(extract_omp_for_data): Renamed to omp_extract_for_data and moved to
      	omp-general.c.
      	(workshare_safe_to_combine_p): Moved to omp-expand.c.
      	(omp_adjust_chunk_size): Likewise.
      	(get_ws_args_for): Likewise.
      	(get_base_type): Removed.
      	(dump_omp_region): Moved to omp-expand.c.
      	(debug_omp_region): Likewise.
      	(debug_all_omp_regions): Likewise.
      	(new_omp_region): Likewise.
      	(free_omp_region_1): Likewise.
      	(free_omp_regions): Renamed to omp_free_regions and moved to
      	omp-expand.c.
      	(find_combined_for): Renamed to omp_find_combined_for, made global.
      	(build_omp_barrier): Renamed to omp_build_barrier and moved to
      	omp-general.c.
      	(omp_max_vf): Moved to omp-general.c.
      	(omp_max_simt_vf): Likewise.
      	(gimple_build_cond_empty): Moved to omp-expand.c.
      	(parallel_needs_hsa_kernel_p): Likewise.
      	(expand_omp_build_assign): Moved declaration to omp-expand.c.
      	(expand_parallel_call): Moved to omp-expand.c.
      	(expand_cilk_for_call): Likewise.
      	(expand_task_call): Likewise.
      	(vec2chain): Likewise.
      	(remove_exit_barrier): Likewise.
      	(remove_exit_barriers): Likewise.
      	(optimize_omp_library_calls): Likewise.
      	(expand_omp_regimplify_p): Likewise.
      	(expand_omp_build_assign): Likewise.
      	(expand_omp_taskreg): Likewise.
      	(oacc_collapse): Likewise.
      	(expand_oacc_collapse_init): Likewise.
      	(expand_oacc_collapse_vars): Likewise.
      	(expand_omp_for_init_counts): Likewise.
      	(expand_omp_for_init_vars): Likewise.
      	(extract_omp_for_update_vars): Likewise.
      	(expand_omp_ordered_source): Likewise.
      	(expand_omp_ordered_sink): Likewise.
      	(expand_omp_ordered_source_sink): Likewise.
      	(expand_omp_for_ordered_loops): Likewise.
      	(expand_omp_for_generic): Likewise.
      	(expand_omp_for_static_nochunk): Likewise.
      	(find_phi_with_arg_on_edge): Likewise.
      	(expand_omp_for_static_chunk): Likewise.
      	(expand_cilk_for): Likewise.
      	(expand_omp_simd): Likewise.
      	(expand_omp_taskloop_for_outer): Likewise.
      	(expand_omp_taskloop_for_inner): Likewise.
      	(expand_oacc_for): Likewise.
      	(expand_omp_for): Likewise.
      	(expand_omp_sections): Likewise.
      	(expand_omp_single): Likewise.
      	(expand_omp_synch): Likewise.
      	(expand_omp_atomic_load): Likewise.
      	(expand_omp_atomic_store): Likewise.
      	(expand_omp_atomic_fetch_op): Likewise.
      	(expand_omp_atomic_pipeline): Likewise.
      	(expand_omp_atomic_mutex): Likewise.
      	(expand_omp_atomic): Likewise.
      	(oacc_launch_pack): and moved to omp-general.c, made public.
      	(OACC_FN_ATTRIB): Likewise.
      	(replace_oacc_fn_attrib): Renamed to oacc_replace_fn_attrib and moved
      	to omp-general.c.
      	(set_oacc_fn_attrib): Renamed to oacc_set_fn_attrib and moved to
      	omp-general.c.
      	(build_oacc_routine_dims): Renamed to oacc_build_routine_dims and
      	moved to omp-general.c.
      	(get_oacc_fn_attrib): Renamed to oacc_get_fn_attrib and moved to
      	omp-general.c.
      	(oacc_fn_attrib_kernels_p): Moved to omp-general.c.
      	(oacc_fn_attrib_level): Moved to omp-offload.c.
      	(get_oacc_fn_dim_size): Renamed to oacc_get_fn_dim_size and moved to
      	omp-general.c.
      	(get_oacc_ifn_dim_arg): Renamed to oacc_get_ifn_dim_arg and moved to
      	omp-general.c.
      	(mark_loops_in_oacc_kernels_region): Moved to omp-expand.c.
      	(grid_launch_attributes_trees): Likewise.
      	(grid_attr_trees): Likewise.
      	(grid_create_kernel_launch_attr_types): Likewise.
      	(grid_insert_store_range_dim): Likewise.
      	(grid_get_kernel_launch_attributes): Likewise.
      	(get_target_argument_identifier_1): Likewise.
      	(get_target_argument_identifier): Likewise.
      	(get_target_argument_value): Likewise.
      	(push_target_argument_according_to_value): Likewise.
      	(get_target_arguments): Likewise.
      	(expand_omp_target): Likewise.
      	(grid_expand_omp_for_loop): Moved to omp-grid.c.
      	(grid_arg_decl_map): Likewise.
      	(grid_remap_kernel_arg_accesses): Likewise.
      	(grid_expand_target_grid_body): Likewise.
      	(expand_omp): Renamed to omp_expand and moved to omp-expand.c.
      	(build_omp_regions_1): Moved to omp-expand.c.
      	(build_omp_regions_root): Likewise.
      	(omp_expand_local): Likewise.
      	(build_omp_regions): Likewise.
      	(execute_expand_omp): Likewise.
      	(pass_data_expand_omp): Likewise.
      	(pass_expand_omp): Likewise.
      	(make_pass_expand_omp): Likewise.
      	(pass_data_expand_omp_ssa): Likewise.
      	(pass_expand_omp_ssa): Likewise.
      	(make_pass_expand_omp_ssa): Likewise.
      	(grid_lastprivate_predicate): Renamed to
      	omp_grid_lastprivate_predicate and moved to omp-grid.c, made public.
      	(grid_prop): Moved to omp-grid.c.
      	(GRID_MISSED_MSG_PREFIX): Likewise.
      	(grid_safe_assignment_p): Likewise.
      	(grid_seq_only_contains_local_assignments): Likewise.
      	(grid_find_single_omp_among_assignments_1): Likewise.
      	(grid_find_single_omp_among_assignments): Likewise.
      	(grid_find_ungridifiable_statement): Likewise.
      	(grid_parallel_clauses_gridifiable): Likewise.
      	(grid_inner_loop_gridifiable_p): Likewise.
      	(grid_dist_follows_simple_pattern): Likewise.
      	(grid_gfor_follows_tiling_pattern): Likewise.
      	(grid_call_permissible_in_distribute_p): Likewise.
      	(grid_handle_call_in_distribute): Likewise.
      	(grid_dist_follows_tiling_pattern): Likewise.
      	(grid_target_follows_gridifiable_pattern): Likewise.
      	(grid_remap_prebody_decls): Likewise.
      	(grid_var_segment): Likewise.
      	(grid_mark_variable_segment): Likewise.
      	(grid_copy_leading_local_assignments): Likewise.
      	(grid_process_grid_body): Likewise.
      	(grid_eliminate_combined_simd_part): Likewise.
      	(grid_mark_tiling_loops): Likewise.
      	(grid_mark_tiling_parallels_and_loops): Likewise.
      	(grid_process_kernel_body_copy): Likewise.
      	(grid_attempt_target_gridification): Likewise.
      	(grid_gridify_all_targets_stmt): Likewise.
      	(grid_gridify_all_targets): Renamed to omp_grid_gridify_all_targets
      	and moved to omp-grid.c, made public.
      	(make_gimple_omp_edges): Renamed to omp_make_gimple_edges and moved to
      	omp-expand.c.
      	(add_decls_addresses_to_decl_constructor): Moved to omp-offload.c.
      	(omp_finish_file): Likewise.
      	(oacc_thread_numbers): Likewise.
      	(oacc_xform_loop): Likewise.
      	(oacc_default_dims, oacc_min_dims): Likewise.
      	(oacc_parse_default_dims): Likewise.
      	(oacc_validate_dims): Likewise.
      	(new_oacc_loop_raw): Likewise.
      	(new_oacc_loop_outer): Likewise.
      	(new_oacc_loop): Likewise.
      	(new_oacc_loop_routine): Likewise.
      	(finish_oacc_loop): Likewise.
      	(free_oacc_loop): Likewise.
      	(dump_oacc_loop_part): Likewise.
      	(dump_oacc_loop): Likewise.
      	(debug_oacc_loop): Likewise.
      	(oacc_loop_discover_walk): Likewise.
      	(oacc_loop_sibling_nreverse): Likewise.
      	(oacc_loop_discovery): Likewise.
      	(oacc_loop_xform_head_tail): Likewise.
      	(oacc_loop_xform_loop): Likewise.
      	(oacc_loop_process): Likewise.
      	(oacc_loop_fixed_partitions): Likewise.
      	(oacc_loop_auto_partitions): Likewise.
      	(oacc_loop_partition): Likewise.
      	(default_goacc_fork_join): Likewise.
      	(default_goacc_reduction): Likewise.
      	(execute_oacc_device_lower): Likewise.
      	(default_goacc_validate_dims): Likewise.
      	(default_goacc_dim_limit): Likewise.
      	(pass_data_oacc_device_lower): Likewise.
      	(pass_oacc_device_lower): Likewise.
      	(make_pass_oacc_device_lower): Likewise.
      	(execute_omp_device_lower): Likewise.
      	(pass_data_omp_device_lower): Likewise.
      	(pass_omp_device_lower): Likewise.
      	(make_pass_omp_device_lower): Likewise.
      	(pass_data_omp_target_link): Likewise.
      	(pass_omp_target_link): Likewise.
      	(find_link_var_op): Likewise.
      	(pass_omp_target_link::execute): Likewise.
      	(make_pass_omp_target_link): Likewise.
      
      	* Makefile.in (OBJS): Added omp-offload.o, omp-expand.o, omp-general.o
      	and omp-grid.o.
      	(GTFILES): Added omp-offload.h, omp-offload.c and omp-expand.c, removed
      	omp-low.h.
      	* gimple-fold.c: Include omp-general.h instead of omp-low.h.
      	(fold_internal_goacc_dim): Adjusted calls to
      	get_oacc_ifn_dim_arg and get_oacc_fn_dim_size to use their new names.
      	* gimplify.c: Include omp-low.h.
      	(omp_notice_variable): Adjust the call to get_oacc_fn_attrib to use
      	its new name.
      	(gimplify_omp_task): Adjusted calls to find_omp_clause to use its new
      	name.
      	(gimplify_omp_for): Likewise.
      	* lto-cgraph.c: Include omp-offload.h instead of omp-low.h.
      	* toplev.c: Include omp-offload.h instead of omp-low.h.
      	* tree-cfg.c: Include omp-general.h instead of omp-low.h.  Also
      	include omp-expand.h.
      	(make_edges_bb): Adjusted the call to make_gimple_omp_edges to use its
      	new name.
      	(make_edges): Adjust the call to free_omp_regions to use its new name.
      	* tree-parloops.c: Include omp-general.h.
      	(create_parallel_loop): Adjusted the call to set_oacc_fn_attrib to use
      	its new name.
      	(parallelize_loops): Adjusted the call to get_oacc_fn_attrib to use
      	its new name.
      	* tree-ssa-loop.c: Include omp-general.h instead of omp-low.h.
      	(gate_oacc_kernels): Adjusted the call to get_oacc_fn_attrib to use
      	its new name.
      	* tree-vrp.c: Include omp-general.h instead of omp-low.h.
      	(extract_range_basic): Adjusted calls to get_oacc_ifn_dim_arg and
      	get_oacc_fn_dim_size to use their new names.
      	* varpool.c: Include omp-offload.h instead of omp-low.h.
      	* gengtype.c (open_base_files): Replace omp-low.h with omp-offload.h in
      	ifiles.
      	* config/nvptx/nvptx.c: Include omp-general.c.
      	(nvptx_expand_call): Adjusted the call to get_oacc_fn_attrib to use
      	its new name.
      	(nvptx_reorg): Likewise.
      	(nvptx_record_offload_symbol): Likewise.
      
      gcc/c-family:
      	* c-omp.c: Include omp-general.h instead of omp-low.h.
      	(c_finish_oacc_wait): Adjusted call to find_omp_clause to use its new
      	name.
      
      gcc/c/
      	* c-parser.c: Include omp-general.h and omp-offload.h instead of
      	omp-low.h.
      	(c_finish_oacc_routine): Adjusted call to
      	get_oacc_fn_attrib, build_oacc_routine_dims and replace_oacc_fn_attrib
      	to use their new names.
      	(c_parser_oacc_enter_exit_data): Adjusted call to find_omp_clause to
      	use its new name.
      	(c_parser_oacc_update): Likewise.
      	(c_parser_omp_simd): Likewise.
      	(c_parser_omp_target_update): Likewise.
      	* c-typeck.c: Include omp-general.h instead of omp-low.h.
      	(c_finish_omp_cancel): Adjusted call to find_omp_clause to use its new
      	name.
      	(c_finish_omp_cancellation_point): Likewise.
      	* gimple-parser.c: Do not include omp-low.h
      
      gcc/cp/
      	* parser.c: Include omp-general.h and omp-offload.h instead of
      	omp-low.h.
      	(cp_parser_omp_simd): Adjusted calls to find_omp_clause to use its new
      	name.
      	(cp_parser_omp_target_update): Likewise.
      	(cp_parser_oacc_declare): Likewise.
      	(cp_parser_oacc_enter_exit_data): Likewise.
      	(cp_parser_oacc_update): Likewise.
      	(cp_finalize_oacc_routine): Adjusted call to get_oacc_fn_attrib,
      	build_oacc_routine_dims and replace_oacc_fn_attrib to use their new
      	names.
      	* semantics.c: Include omp-general insteda of omp-low.h.
      	(finish_omp_for): Adjusted calls to find_omp_clause to use its new
      	name.
      	(finish_omp_cancel): Likewise.
      	(finish_omp_cancellation_point): Likewise.
      
      fortran/
      	* trans-openmp.c: Include omp-general.h.
      
      From-SVN: r243673
      Martin Jambor committed