1========================= 2Clang Language Extensions 3========================= 4 5.. contents:: 6 :local: 7 :depth: 1 8 9.. toctree:: 10 :hidden: 11 12 ObjectiveCLiterals 13 BlockLanguageSpec 14 Block-ABI-Apple 15 AutomaticReferenceCounting 16 17Introduction 18============ 19 20This document describes the language extensions provided by Clang. In addition 21to the language extensions listed here, Clang aims to support a broad range of 22GCC extensions. Please see the `GCC manual 23<http://gcc.gnu.org/onlinedocs/gcc/C-Extensions.html>`_ for more information on 24these extensions. 25 26.. _langext-feature_check: 27 28Feature Checking Macros 29======================= 30 31Language extensions can be very useful, but only if you know you can depend on 32them. In order to allow fine-grain features checks, we support three builtin 33function-like macros. This allows you to directly test for a feature in your 34code without having to resort to something like autoconf or fragile "compiler 35version checks". 36 37``__has_builtin`` 38----------------- 39 40This function-like macro takes a single identifier argument that is the name of 41a builtin function. It evaluates to 1 if the builtin is supported or 0 if not. 42It can be used like this: 43 44.. code-block:: c++ 45 46 #ifndef __has_builtin // Optional of course. 47 #define __has_builtin(x) 0 // Compatibility with non-clang compilers. 48 #endif 49 50 ... 51 #if __has_builtin(__builtin_trap) 52 __builtin_trap(); 53 #else 54 abort(); 55 #endif 56 ... 57 58.. _langext-__has_feature-__has_extension: 59 60``__has_feature`` and ``__has_extension`` 61----------------------------------------- 62 63These function-like macros take a single identifier argument that is the name 64of a feature. ``__has_feature`` evaluates to 1 if the feature is both 65supported by Clang and standardized in the current language standard or 0 if 66not (but see :ref:`below <langext-has-feature-back-compat>`), while 67``__has_extension`` evaluates to 1 if the feature is supported by Clang in the 68current language (either as a language extension or a standard language 69feature) or 0 if not. They can be used like this: 70 71.. code-block:: c++ 72 73 #ifndef __has_feature // Optional of course. 74 #define __has_feature(x) 0 // Compatibility with non-clang compilers. 75 #endif 76 #ifndef __has_extension 77 #define __has_extension __has_feature // Compatibility with pre-3.0 compilers. 78 #endif 79 80 ... 81 #if __has_feature(cxx_rvalue_references) 82 // This code will only be compiled with the -std=c++11 and -std=gnu++11 83 // options, because rvalue references are only standardized in C++11. 84 #endif 85 86 #if __has_extension(cxx_rvalue_references) 87 // This code will be compiled with the -std=c++11, -std=gnu++11, -std=c++98 88 // and -std=gnu++98 options, because rvalue references are supported as a 89 // language extension in C++98. 90 #endif 91 92.. _langext-has-feature-back-compat: 93 94For backwards compatibility reasons, ``__has_feature`` can also be used to test 95for support for non-standardized features, i.e. features not prefixed ``c_``, 96``cxx_`` or ``objc_``. 97 98Another use of ``__has_feature`` is to check for compiler features not related 99to the language standard, such as e.g. :doc:`AddressSanitizer 100<AddressSanitizer>`. 101 102If the ``-pedantic-errors`` option is given, ``__has_extension`` is equivalent 103to ``__has_feature``. 104 105The feature tag is described along with the language feature below. 106 107The feature name or extension name can also be specified with a preceding and 108following ``__`` (double underscore) to avoid interference from a macro with 109the same name. For instance, ``__cxx_rvalue_references__`` can be used instead 110of ``cxx_rvalue_references``. 111 112``__has_attribute`` 113------------------- 114 115This function-like macro takes a single identifier argument that is the name of 116an attribute. It evaluates to 1 if the attribute is supported by the current 117compilation target, or 0 if not. It can be used like this: 118 119.. code-block:: c++ 120 121 #ifndef __has_attribute // Optional of course. 122 #define __has_attribute(x) 0 // Compatibility with non-clang compilers. 123 #endif 124 125 ... 126 #if __has_attribute(always_inline) 127 #define ALWAYS_INLINE __attribute__((always_inline)) 128 #else 129 #define ALWAYS_INLINE 130 #endif 131 ... 132 133The attribute name can also be specified with a preceding and following ``__`` 134(double underscore) to avoid interference from a macro with the same name. For 135instance, ``__always_inline__`` can be used instead of ``always_inline``. 136 137 138Include File Checking Macros 139============================ 140 141Not all developments systems have the same include files. The 142:ref:`langext-__has_include` and :ref:`langext-__has_include_next` macros allow 143you to check for the existence of an include file before doing a possibly 144failing ``#include`` directive. Include file checking macros must be used 145as expressions in ``#if`` or ``#elif`` preprocessing directives. 146 147.. _langext-__has_include: 148 149``__has_include`` 150----------------- 151 152This function-like macro takes a single file name string argument that is the 153name of an include file. It evaluates to 1 if the file can be found using the 154include paths, or 0 otherwise: 155 156.. code-block:: c++ 157 158 // Note the two possible file name string formats. 159 #if __has_include("myinclude.h") && __has_include(<stdint.h>) 160 # include "myinclude.h" 161 #endif 162 163To test for this feature, use ``#if defined(__has_include)``: 164 165.. code-block:: c++ 166 167 // To avoid problem with non-clang compilers not having this macro. 168 #if defined(__has_include) 169 #if __has_include("myinclude.h") 170 # include "myinclude.h" 171 #endif 172 #endif 173 174.. _langext-__has_include_next: 175 176``__has_include_next`` 177---------------------- 178 179This function-like macro takes a single file name string argument that is the 180name of an include file. It is like ``__has_include`` except that it looks for 181the second instance of the given file found in the include paths. It evaluates 182to 1 if the second instance of the file can be found using the include paths, 183or 0 otherwise: 184 185.. code-block:: c++ 186 187 // Note the two possible file name string formats. 188 #if __has_include_next("myinclude.h") && __has_include_next(<stdint.h>) 189 # include_next "myinclude.h" 190 #endif 191 192 // To avoid problem with non-clang compilers not having this macro. 193 #if defined(__has_include_next) 194 #if __has_include_next("myinclude.h") 195 # include_next "myinclude.h" 196 #endif 197 #endif 198 199Note that ``__has_include_next``, like the GNU extension ``#include_next`` 200directive, is intended for use in headers only, and will issue a warning if 201used in the top-level compilation file. A warning will also be issued if an 202absolute path is used in the file argument. 203 204``__has_warning`` 205----------------- 206 207This function-like macro takes a string literal that represents a command line 208option for a warning and returns true if that is a valid warning option. 209 210.. code-block:: c++ 211 212 #if __has_warning("-Wformat") 213 ... 214 #endif 215 216Builtin Macros 217============== 218 219``__BASE_FILE__`` 220 Defined to a string that contains the name of the main input file passed to 221 Clang. 222 223``__COUNTER__`` 224 Defined to an integer value that starts at zero and is incremented each time 225 the ``__COUNTER__`` macro is expanded. 226 227``__INCLUDE_LEVEL__`` 228 Defined to an integral value that is the include depth of the file currently 229 being translated. For the main file, this value is zero. 230 231``__TIMESTAMP__`` 232 Defined to the date and time of the last modification of the current source 233 file. 234 235``__clang__`` 236 Defined when compiling with Clang 237 238``__clang_major__`` 239 Defined to the major marketing version number of Clang (e.g., the 2 in 240 2.0.1). Note that marketing version numbers should not be used to check for 241 language features, as different vendors use different numbering schemes. 242 Instead, use the :ref:`langext-feature_check`. 243 244``__clang_minor__`` 245 Defined to the minor version number of Clang (e.g., the 0 in 2.0.1). Note 246 that marketing version numbers should not be used to check for language 247 features, as different vendors use different numbering schemes. Instead, use 248 the :ref:`langext-feature_check`. 249 250``__clang_patchlevel__`` 251 Defined to the marketing patch level of Clang (e.g., the 1 in 2.0.1). 252 253``__clang_version__`` 254 Defined to a string that captures the Clang marketing version, including the 255 Subversion tag or revision number, e.g., "``1.5 (trunk 102332)``". 256 257.. _langext-vectors: 258 259Vectors and Extended Vectors 260============================ 261 262Supports the GCC, OpenCL, AltiVec and NEON vector extensions. 263 264OpenCL vector types are created using ``ext_vector_type`` attribute. It 265support for ``V.xyzw`` syntax and other tidbits as seen in OpenCL. An example 266is: 267 268.. code-block:: c++ 269 270 typedef float float4 __attribute__((ext_vector_type(4))); 271 typedef float float2 __attribute__((ext_vector_type(2))); 272 273 float4 foo(float2 a, float2 b) { 274 float4 c; 275 c.xz = a; 276 c.yw = b; 277 return c; 278 } 279 280Query for this feature with ``__has_extension(attribute_ext_vector_type)``. 281 282Giving ``-faltivec`` option to clang enables support for AltiVec vector syntax 283and functions. For example: 284 285.. code-block:: c++ 286 287 vector float foo(vector int a) { 288 vector int b; 289 b = vec_add(a, a) + a; 290 return (vector float)b; 291 } 292 293NEON vector types are created using ``neon_vector_type`` and 294``neon_polyvector_type`` attributes. For example: 295 296.. code-block:: c++ 297 298 typedef __attribute__((neon_vector_type(8))) int8_t int8x8_t; 299 typedef __attribute__((neon_polyvector_type(16))) poly8_t poly8x16_t; 300 301 int8x8_t foo(int8x8_t a) { 302 int8x8_t v; 303 v = a; 304 return v; 305 } 306 307Vector Literals 308--------------- 309 310Vector literals can be used to create vectors from a set of scalars, or 311vectors. Either parentheses or braces form can be used. In the parentheses 312form the number of literal values specified must be one, i.e. referring to a 313scalar value, or must match the size of the vector type being created. If a 314single scalar literal value is specified, the scalar literal value will be 315replicated to all the components of the vector type. In the brackets form any 316number of literals can be specified. For example: 317 318.. code-block:: c++ 319 320 typedef int v4si __attribute__((__vector_size__(16))); 321 typedef float float4 __attribute__((ext_vector_type(4))); 322 typedef float float2 __attribute__((ext_vector_type(2))); 323 324 v4si vsi = (v4si){1, 2, 3, 4}; 325 float4 vf = (float4)(1.0f, 2.0f, 3.0f, 4.0f); 326 vector int vi1 = (vector int)(1); // vi1 will be (1, 1, 1, 1). 327 vector int vi2 = (vector int){1}; // vi2 will be (1, 0, 0, 0). 328 vector int vi3 = (vector int)(1, 2); // error 329 vector int vi4 = (vector int){1, 2}; // vi4 will be (1, 2, 0, 0). 330 vector int vi5 = (vector int)(1, 2, 3, 4); 331 float4 vf = (float4)((float2)(1.0f, 2.0f), (float2)(3.0f, 4.0f)); 332 333Vector Operations 334----------------- 335 336The table below shows the support for each operation by vector extension. A 337dash indicates that an operation is not accepted according to a corresponding 338specification. 339 340============================== ====== ======= === ==== 341 Opeator OpenCL AltiVec GCC NEON 342============================== ====== ======= === ==== 343[] yes yes yes -- 344unary operators +, -- yes yes yes -- 345++, -- -- yes yes yes -- 346+,--,*,/,% yes yes yes -- 347bitwise operators &,|,^,~ yes yes yes -- 348>>,<< yes yes yes -- 349!, &&, || no -- -- -- 350==, !=, >, <, >=, <= yes yes -- -- 351= yes yes yes yes 352:? yes -- -- -- 353sizeof yes yes yes yes 354============================== ====== ======= === ==== 355 356See also :ref:`langext-__builtin_shufflevector`. 357 358Messages on ``deprecated`` and ``unavailable`` Attributes 359========================================================= 360 361An optional string message can be added to the ``deprecated`` and 362``unavailable`` attributes. For example: 363 364.. code-block:: c++ 365 366 void explode(void) __attribute__((deprecated("extremely unsafe, use 'combust' instead!!!"))); 367 368If the deprecated or unavailable declaration is used, the message will be 369incorporated into the appropriate diagnostic: 370 371.. code-block:: c++ 372 373 harmless.c:4:3: warning: 'explode' is deprecated: extremely unsafe, use 'combust' instead!!! 374 [-Wdeprecated-declarations] 375 explode(); 376 ^ 377 378Query for this feature with 379``__has_extension(attribute_deprecated_with_message)`` and 380``__has_extension(attribute_unavailable_with_message)``. 381 382Attributes on Enumerators 383========================= 384 385Clang allows attributes to be written on individual enumerators. This allows 386enumerators to be deprecated, made unavailable, etc. The attribute must appear 387after the enumerator name and before any initializer, like so: 388 389.. code-block:: c++ 390 391 enum OperationMode { 392 OM_Invalid, 393 OM_Normal, 394 OM_Terrified __attribute__((deprecated)), 395 OM_AbortOnError __attribute__((deprecated)) = 4 396 }; 397 398Attributes on the ``enum`` declaration do not apply to individual enumerators. 399 400Query for this feature with ``__has_extension(enumerator_attributes)``. 401 402'User-Specified' System Frameworks 403================================== 404 405Clang provides a mechanism by which frameworks can be built in such a way that 406they will always be treated as being "system frameworks", even if they are not 407present in a system framework directory. This can be useful to system 408framework developers who want to be able to test building other applications 409with development builds of their framework, including the manner in which the 410compiler changes warning behavior for system headers. 411 412Framework developers can opt-in to this mechanism by creating a 413"``.system_framework``" file at the top-level of their framework. That is, the 414framework should have contents like: 415 416.. code-block:: none 417 418 .../TestFramework.framework 419 .../TestFramework.framework/.system_framework 420 .../TestFramework.framework/Headers 421 .../TestFramework.framework/Headers/TestFramework.h 422 ... 423 424Clang will treat the presence of this file as an indicator that the framework 425should be treated as a system framework, regardless of how it was found in the 426framework search path. For consistency, we recommend that such files never be 427included in installed versions of the framework. 428 429Availability attribute 430====================== 431 432Clang introduces the ``availability`` attribute, which can be placed on 433declarations to describe the lifecycle of that declaration relative to 434operating system versions. Consider the function declaration for a 435hypothetical function ``f``: 436 437.. code-block:: c++ 438 439 void f(void) __attribute__((availability(macosx,introduced=10.4,deprecated=10.6,obsoleted=10.7))); 440 441The availability attribute states that ``f`` was introduced in Mac OS X 10.4, 442deprecated in Mac OS X 10.6, and obsoleted in Mac OS X 10.7. This information 443is used by Clang to determine when it is safe to use ``f``: for example, if 444Clang is instructed to compile code for Mac OS X 10.5, a call to ``f()`` 445succeeds. If Clang is instructed to compile code for Mac OS X 10.6, the call 446succeeds but Clang emits a warning specifying that the function is deprecated. 447Finally, if Clang is instructed to compile code for Mac OS X 10.7, the call 448fails because ``f()`` is no longer available. 449 450The availability attribute is a comma-separated list starting with the 451platform name and then including clauses specifying important milestones in the 452declaration's lifetime (in any order) along with additional information. Those 453clauses can be: 454 455introduced=\ *version* 456 The first version in which this declaration was introduced. 457 458deprecated=\ *version* 459 The first version in which this declaration was deprecated, meaning that 460 users should migrate away from this API. 461 462obsoleted=\ *version* 463 The first version in which this declaration was obsoleted, meaning that it 464 was removed completely and can no longer be used. 465 466unavailable 467 This declaration is never available on this platform. 468 469message=\ *string-literal* 470 Additional message text that Clang will provide when emitting a warning or 471 error about use of a deprecated or obsoleted declaration. Useful to direct 472 users to replacement APIs. 473 474Multiple availability attributes can be placed on a declaration, which may 475correspond to different platforms. Only the availability attribute with the 476platform corresponding to the target platform will be used; any others will be 477ignored. If no availability attribute specifies availability for the current 478target platform, the availability attributes are ignored. Supported platforms 479are: 480 481``ios`` 482 Apple's iOS operating system. The minimum deployment target is specified by 483 the ``-mios-version-min=*version*`` or ``-miphoneos-version-min=*version*`` 484 command-line arguments. 485 486``macosx`` 487 Apple's Mac OS X operating system. The minimum deployment target is 488 specified by the ``-mmacosx-version-min=*version*`` command-line argument. 489 490A declaration can be used even when deploying back to a platform version prior 491to when the declaration was introduced. When this happens, the declaration is 492`weakly linked 493<https://developer.apple.com/library/mac/#documentation/MacOSX/Conceptual/BPFrameworks/Concepts/WeakLinking.html>`_, 494as if the ``weak_import`` attribute were added to the declaration. A 495weakly-linked declaration may or may not be present a run-time, and a program 496can determine whether the declaration is present by checking whether the 497address of that declaration is non-NULL. 498 499If there are multiple declarations of the same entity, the availability 500attributes must either match on a per-platform basis or later 501declarations must not have availability attributes for that 502platform. For example: 503 504.. code-block:: c 505 506 void g(void) __attribute__((availability(macosx,introduced=10.4))); 507 void g(void) __attribute__((availability(macosx,introduced=10.4))); // okay, matches 508 void g(void) __attribute__((availability(ios,introduced=4.0))); // okay, adds a new platform 509 void g(void); // okay, inherits both macosx and ios availability from above. 510 void g(void) __attribute__((availability(macosx,introduced=10.5))); // error: mismatch 511 512When one method overrides another, the overriding method can be more widely available than the overridden method, e.g.,: 513 514.. code-block:: objc 515 516 @interface A 517 - (id)method __attribute__((availability(macosx,introduced=10.4))); 518 - (id)method2 __attribute__((availability(macosx,introduced=10.4))); 519 @end 520 521 @interface B : A 522 - (id)method __attribute__((availability(macosx,introduced=10.3))); // okay: method moved into base class later 523 - (id)method __attribute__((availability(macosx,introduced=10.5))); // error: this method was available via the base class in 10.4 524 @end 525 526Checks for Standard Language Features 527===================================== 528 529The ``__has_feature`` macro can be used to query if certain standard language 530features are enabled. The ``__has_extension`` macro can be used to query if 531language features are available as an extension when compiling for a standard 532which does not provide them. The features which can be tested are listed here. 533 534C++98 535----- 536 537The features listed below are part of the C++98 standard. These features are 538enabled by default when compiling C++ code. 539 540C++ exceptions 541^^^^^^^^^^^^^^ 542 543Use ``__has_feature(cxx_exceptions)`` to determine if C++ exceptions have been 544enabled. For example, compiling code with ``-fno-exceptions`` disables C++ 545exceptions. 546 547C++ RTTI 548^^^^^^^^ 549 550Use ``__has_feature(cxx_rtti)`` to determine if C++ RTTI has been enabled. For 551example, compiling code with ``-fno-rtti`` disables the use of RTTI. 552 553C++11 554----- 555 556The features listed below are part of the C++11 standard. As a result, all 557these features are enabled with the ``-std=c++11`` or ``-std=gnu++11`` option 558when compiling C++ code. 559 560C++11 SFINAE includes access control 561^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 562 563Use ``__has_feature(cxx_access_control_sfinae)`` or 564``__has_extension(cxx_access_control_sfinae)`` to determine whether 565access-control errors (e.g., calling a private constructor) are considered to 566be template argument deduction errors (aka SFINAE errors), per `C++ DR1170 567<http://www.open-std.org/jtc1/sc22/wg21/docs/cwg_defects.html#1170>`_. 568 569C++11 alias templates 570^^^^^^^^^^^^^^^^^^^^^ 571 572Use ``__has_feature(cxx_alias_templates)`` or 573``__has_extension(cxx_alias_templates)`` to determine if support for C++11's 574alias declarations and alias templates is enabled. 575 576C++11 alignment specifiers 577^^^^^^^^^^^^^^^^^^^^^^^^^^ 578 579Use ``__has_feature(cxx_alignas)`` or ``__has_extension(cxx_alignas)`` to 580determine if support for alignment specifiers using ``alignas`` is enabled. 581 582C++11 attributes 583^^^^^^^^^^^^^^^^ 584 585Use ``__has_feature(cxx_attributes)`` or ``__has_extension(cxx_attributes)`` to 586determine if support for attribute parsing with C++11's square bracket notation 587is enabled. 588 589C++11 generalized constant expressions 590^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 591 592Use ``__has_feature(cxx_constexpr)`` to determine if support for generalized 593constant expressions (e.g., ``constexpr``) is enabled. 594 595C++11 ``decltype()`` 596^^^^^^^^^^^^^^^^^^^^ 597 598Use ``__has_feature(cxx_decltype)`` or ``__has_extension(cxx_decltype)`` to 599determine if support for the ``decltype()`` specifier is enabled. C++11's 600``decltype`` does not require type-completeness of a function call expression. 601Use ``__has_feature(cxx_decltype_incomplete_return_types)`` or 602``__has_extension(cxx_decltype_incomplete_return_types)`` to determine if 603support for this feature is enabled. 604 605C++11 default template arguments in function templates 606^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 607 608Use ``__has_feature(cxx_default_function_template_args)`` or 609``__has_extension(cxx_default_function_template_args)`` to determine if support 610for default template arguments in function templates is enabled. 611 612C++11 ``default``\ ed functions 613^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 614 615Use ``__has_feature(cxx_defaulted_functions)`` or 616``__has_extension(cxx_defaulted_functions)`` to determine if support for 617defaulted function definitions (with ``= default``) is enabled. 618 619C++11 delegating constructors 620^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 621 622Use ``__has_feature(cxx_delegating_constructors)`` to determine if support for 623delegating constructors is enabled. 624 625C++11 ``deleted`` functions 626^^^^^^^^^^^^^^^^^^^^^^^^^^^ 627 628Use ``__has_feature(cxx_deleted_functions)`` or 629``__has_extension(cxx_deleted_functions)`` to determine if support for deleted 630function definitions (with ``= delete``) is enabled. 631 632C++11 explicit conversion functions 633^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 634 635Use ``__has_feature(cxx_explicit_conversions)`` to determine if support for 636``explicit`` conversion functions is enabled. 637 638C++11 generalized initializers 639^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 640 641Use ``__has_feature(cxx_generalized_initializers)`` to determine if support for 642generalized initializers (using braced lists and ``std::initializer_list``) is 643enabled. 644 645C++11 implicit move constructors/assignment operators 646^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 647 648Use ``__has_feature(cxx_implicit_moves)`` to determine if Clang will implicitly 649generate move constructors and move assignment operators where needed. 650 651C++11 inheriting constructors 652^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 653 654Use ``__has_feature(cxx_inheriting_constructors)`` to determine if support for 655inheriting constructors is enabled. 656 657C++11 inline namespaces 658^^^^^^^^^^^^^^^^^^^^^^^ 659 660Use ``__has_feature(cxx_inline_namespaces)`` or 661``__has_extension(cxx_inline_namespaces)`` to determine if support for inline 662namespaces is enabled. 663 664C++11 lambdas 665^^^^^^^^^^^^^ 666 667Use ``__has_feature(cxx_lambdas)`` or ``__has_extension(cxx_lambdas)`` to 668determine if support for lambdas is enabled. 669 670C++11 local and unnamed types as template arguments 671^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 672 673Use ``__has_feature(cxx_local_type_template_args)`` or 674``__has_extension(cxx_local_type_template_args)`` to determine if support for 675local and unnamed types as template arguments is enabled. 676 677C++11 noexcept 678^^^^^^^^^^^^^^ 679 680Use ``__has_feature(cxx_noexcept)`` or ``__has_extension(cxx_noexcept)`` to 681determine if support for noexcept exception specifications is enabled. 682 683C++11 in-class non-static data member initialization 684^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 685 686Use ``__has_feature(cxx_nonstatic_member_init)`` to determine whether in-class 687initialization of non-static data members is enabled. 688 689C++11 ``nullptr`` 690^^^^^^^^^^^^^^^^^ 691 692Use ``__has_feature(cxx_nullptr)`` or ``__has_extension(cxx_nullptr)`` to 693determine if support for ``nullptr`` is enabled. 694 695C++11 ``override control`` 696^^^^^^^^^^^^^^^^^^^^^^^^^^ 697 698Use ``__has_feature(cxx_override_control)`` or 699``__has_extension(cxx_override_control)`` to determine if support for the 700override control keywords is enabled. 701 702C++11 reference-qualified functions 703^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 704 705Use ``__has_feature(cxx_reference_qualified_functions)`` or 706``__has_extension(cxx_reference_qualified_functions)`` to determine if support 707for reference-qualified functions (e.g., member functions with ``&`` or ``&&`` 708applied to ``*this``) is enabled. 709 710C++11 range-based ``for`` loop 711^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 712 713Use ``__has_feature(cxx_range_for)`` or ``__has_extension(cxx_range_for)`` to 714determine if support for the range-based for loop is enabled. 715 716C++11 raw string literals 717^^^^^^^^^^^^^^^^^^^^^^^^^ 718 719Use ``__has_feature(cxx_raw_string_literals)`` to determine if support for raw 720string literals (e.g., ``R"x(foo\bar)x"``) is enabled. 721 722C++11 rvalue references 723^^^^^^^^^^^^^^^^^^^^^^^ 724 725Use ``__has_feature(cxx_rvalue_references)`` or 726``__has_extension(cxx_rvalue_references)`` to determine if support for rvalue 727references is enabled. 728 729C++11 ``static_assert()`` 730^^^^^^^^^^^^^^^^^^^^^^^^^ 731 732Use ``__has_feature(cxx_static_assert)`` or 733``__has_extension(cxx_static_assert)`` to determine if support for compile-time 734assertions using ``static_assert`` is enabled. 735 736C++11 ``thread_local`` 737^^^^^^^^^^^^^^^^^^^^^^ 738 739Use ``__has_feature(cxx_thread_local)`` to determine if support for 740``thread_local`` variables is enabled. 741 742C++11 type inference 743^^^^^^^^^^^^^^^^^^^^ 744 745Use ``__has_feature(cxx_auto_type)`` or ``__has_extension(cxx_auto_type)`` to 746determine C++11 type inference is supported using the ``auto`` specifier. If 747this is disabled, ``auto`` will instead be a storage class specifier, as in C 748or C++98. 749 750C++11 strongly typed enumerations 751^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 752 753Use ``__has_feature(cxx_strong_enums)`` or 754``__has_extension(cxx_strong_enums)`` to determine if support for strongly 755typed, scoped enumerations is enabled. 756 757C++11 trailing return type 758^^^^^^^^^^^^^^^^^^^^^^^^^^ 759 760Use ``__has_feature(cxx_trailing_return)`` or 761``__has_extension(cxx_trailing_return)`` to determine if support for the 762alternate function declaration syntax with trailing return type is enabled. 763 764C++11 Unicode string literals 765^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 766 767Use ``__has_feature(cxx_unicode_literals)`` to determine if support for Unicode 768string literals is enabled. 769 770C++11 unrestricted unions 771^^^^^^^^^^^^^^^^^^^^^^^^^ 772 773Use ``__has_feature(cxx_unrestricted_unions)`` to determine if support for 774unrestricted unions is enabled. 775 776C++11 user-defined literals 777^^^^^^^^^^^^^^^^^^^^^^^^^^^ 778 779Use ``__has_feature(cxx_user_literals)`` to determine if support for 780user-defined literals is enabled. 781 782C++11 variadic templates 783^^^^^^^^^^^^^^^^^^^^^^^^ 784 785Use ``__has_feature(cxx_variadic_templates)`` or 786``__has_extension(cxx_variadic_templates)`` to determine if support for 787variadic templates is enabled. 788 789C++1y 790----- 791 792The features listed below are part of the committee draft for the C++1y 793standard. As a result, all these features are enabled with the ``-std=c++1y`` 794or ``-std=gnu++1y`` option when compiling C++ code. 795 796C++1y binary literals 797^^^^^^^^^^^^^^^^^^^^^ 798 799Use ``__has_feature(cxx_binary_literals)`` or 800``__has_extension(cxx_binary_literals)`` to determine whether 801binary literals (for instance, ``0b10010``) are recognized. Clang supports this 802feature as an extension in all language modes. 803 804C++1y contextual conversions 805^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 806 807Use ``__has_feature(cxx_contextual_conversions)`` or 808``__has_extension(cxx_contextual_conversions)`` to determine if the C++1y rules 809are used when performing an implicit conversion for an array bound in a 810*new-expression*, the operand of a *delete-expression*, an integral constant 811expression, or a condition in a ``switch`` statement. 812 813C++1y decltype(auto) 814^^^^^^^^^^^^^^^^^^^^ 815 816Use ``__has_feature(cxx_decltype_auto)`` or 817``__has_extension(cxx_decltype_auto)`` to determine if support 818for the ``decltype(auto)`` placeholder type is enabled. 819 820C++1y default initializers for aggregates 821^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 822 823Use ``__has_feature(cxx_aggregate_nsdmi)`` or 824``__has_extension(cxx_aggregate_nsdmi)`` to determine if support 825for default initializers in aggregate members is enabled. 826 827C++1y generalized lambda capture 828^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 829 830Use ``__has_feature(cxx_init_capture)`` or 831``__has_extension(cxx_init_capture)`` to determine if support for 832lambda captures with explicit initializers is enabled 833(for instance, ``[n(0)] { return ++n; }``). 834 835C++1y generic lambdas 836^^^^^^^^^^^^^^^^^^^^^ 837 838Use ``__has_feature(cxx_generic_lambda)`` or 839``__has_extension(cxx_generic_lambda)`` to determine if support for generic 840(polymorphic) lambdas is enabled 841(for instance, ``[] (auto x) { return x + 1; }``). 842 843C++1y relaxed constexpr 844^^^^^^^^^^^^^^^^^^^^^^^ 845 846Use ``__has_feature(cxx_relaxed_constexpr)`` or 847``__has_extension(cxx_relaxed_constexpr)`` to determine if variable 848declarations, local variable modification, and control flow constructs 849are permitted in ``constexpr`` functions. 850 851C++1y return type deduction 852^^^^^^^^^^^^^^^^^^^^^^^^^^^ 853 854Use ``__has_feature(cxx_return_type_deduction)`` or 855``__has_extension(cxx_return_type_deduction)`` to determine if support 856for return type deduction for functions (using ``auto`` as a return type) 857is enabled. 858 859C++1y runtime-sized arrays 860^^^^^^^^^^^^^^^^^^^^^^^^^^ 861 862Use ``__has_feature(cxx_runtime_array)`` or 863``__has_extension(cxx_runtime_array)`` to determine if support 864for arrays of runtime bound (a restricted form of variable-length arrays) 865is enabled. 866Clang's implementation of this feature is incomplete. 867 868C++1y variable templates 869^^^^^^^^^^^^^^^^^^^^^^^^ 870 871Use ``__has_feature(cxx_variable_templates)`` or 872``__has_extension(cxx_variable_templates)`` to determine if support for 873templated variable declarations is enabled. 874 875C11 876--- 877 878The features listed below are part of the C11 standard. As a result, all these 879features are enabled with the ``-std=c11`` or ``-std=gnu11`` option when 880compiling C code. Additionally, because these features are all 881backward-compatible, they are available as extensions in all language modes. 882 883C11 alignment specifiers 884^^^^^^^^^^^^^^^^^^^^^^^^ 885 886Use ``__has_feature(c_alignas)`` or ``__has_extension(c_alignas)`` to determine 887if support for alignment specifiers using ``_Alignas`` is enabled. 888 889C11 atomic operations 890^^^^^^^^^^^^^^^^^^^^^ 891 892Use ``__has_feature(c_atomic)`` or ``__has_extension(c_atomic)`` to determine 893if support for atomic types using ``_Atomic`` is enabled. Clang also provides 894:ref:`a set of builtins <langext-__c11_atomic>` which can be used to implement 895the ``<stdatomic.h>`` operations on ``_Atomic`` types. 896 897C11 generic selections 898^^^^^^^^^^^^^^^^^^^^^^ 899 900Use ``__has_feature(c_generic_selections)`` or 901``__has_extension(c_generic_selections)`` to determine if support for generic 902selections is enabled. 903 904As an extension, the C11 generic selection expression is available in all 905languages supported by Clang. The syntax is the same as that given in the C11 906standard. 907 908In C, type compatibility is decided according to the rules given in the 909appropriate standard, but in C++, which lacks the type compatibility rules used 910in C, types are considered compatible only if they are equivalent. 911 912C11 ``_Static_assert()`` 913^^^^^^^^^^^^^^^^^^^^^^^^ 914 915Use ``__has_feature(c_static_assert)`` or ``__has_extension(c_static_assert)`` 916to determine if support for compile-time assertions using ``_Static_assert`` is 917enabled. 918 919C11 ``_Thread_local`` 920^^^^^^^^^^^^^^^^^^^^^ 921 922Use ``__has_feature(c_thread_local)`` or ``__has_extension(c_thread_local)`` 923to determine if support for ``_Thread_local`` variables is enabled. 924 925Checks for Type Trait Primitives 926================================ 927 928Type trait primitives are special builtin constant expressions that can be used 929by the standard C++ library to facilitate or simplify the implementation of 930user-facing type traits in the <type_traits> header. 931 932They are not intended to be used directly by user code because they are 933implementation-defined and subject to change -- as such they're tied closely to 934the supported set of system headers, currently: 935 936* LLVM's own libc++ 937* GNU libstdc++ 938* The Microsoft standard C++ library 939 940Clang supports the `GNU C++ type traits 941<http://gcc.gnu.org/onlinedocs/gcc/Type-Traits.html>`_ and a subset of the 942`Microsoft Visual C++ Type traits 943<http://msdn.microsoft.com/en-us/library/ms177194(v=VS.100).aspx>`_. 944 945Feature detection is supported only for some of the primitives at present. User 946code should not use these checks because they bear no direct relation to the 947actual set of type traits supported by the C++ standard library. 948 949For type trait ``__X``, ``__has_extension(X)`` indicates the presence of the 950type trait primitive in the compiler. A simplistic usage example as might be 951seen in standard C++ headers follows: 952 953.. code-block:: c++ 954 955 #if __has_extension(is_convertible_to) 956 template<typename From, typename To> 957 struct is_convertible_to { 958 static const bool value = __is_convertible_to(From, To); 959 }; 960 #else 961 // Emulate type trait for compatibility with other compilers. 962 #endif 963 964The following type trait primitives are supported by Clang: 965 966* ``__has_nothrow_assign`` (GNU, Microsoft) 967* ``__has_nothrow_copy`` (GNU, Microsoft) 968* ``__has_nothrow_constructor`` (GNU, Microsoft) 969* ``__has_trivial_assign`` (GNU, Microsoft) 970* ``__has_trivial_copy`` (GNU, Microsoft) 971* ``__has_trivial_constructor`` (GNU, Microsoft) 972* ``__has_trivial_destructor`` (GNU, Microsoft) 973* ``__has_virtual_destructor`` (GNU, Microsoft) 974* ``__is_abstract`` (GNU, Microsoft) 975* ``__is_base_of`` (GNU, Microsoft) 976* ``__is_class`` (GNU, Microsoft) 977* ``__is_convertible_to`` (Microsoft) 978* ``__is_empty`` (GNU, Microsoft) 979* ``__is_enum`` (GNU, Microsoft) 980* ``__is_interface_class`` (Microsoft) 981* ``__is_pod`` (GNU, Microsoft) 982* ``__is_polymorphic`` (GNU, Microsoft) 983* ``__is_union`` (GNU, Microsoft) 984* ``__is_literal(type)``: Determines whether the given type is a literal type 985* ``__is_final``: Determines whether the given type is declared with a 986 ``final`` class-virt-specifier. 987* ``__underlying_type(type)``: Retrieves the underlying type for a given 988 ``enum`` type. This trait is required to implement the C++11 standard 989 library. 990* ``__is_trivially_assignable(totype, fromtype)``: Determines whether a value 991 of type ``totype`` can be assigned to from a value of type ``fromtype`` such 992 that no non-trivial functions are called as part of that assignment. This 993 trait is required to implement the C++11 standard library. 994* ``__is_trivially_constructible(type, argtypes...)``: Determines whether a 995 value of type ``type`` can be direct-initialized with arguments of types 996 ``argtypes...`` such that no non-trivial functions are called as part of 997 that initialization. This trait is required to implement the C++11 standard 998 library. 999* ``__is_destructible`` (MSVC 2013): partially implemented 1000* ``__is_nothrow_destructible`` (MSVC 2013): partially implemented 1001* ``__is_nothrow_assignable`` (MSVC 2013, clang) 1002* ``__is_constructible`` (MSVC 2013, clang) 1003* ``__is_nothrow_constructible`` (MSVC 2013, clang) 1004 1005Blocks 1006====== 1007 1008The syntax and high level language feature description is in 1009:doc:`BlockLanguageSpec<BlockLanguageSpec>`. Implementation and ABI details for 1010the clang implementation are in :doc:`Block-ABI-Apple<Block-ABI-Apple>`. 1011 1012Query for this feature with ``__has_extension(blocks)``. 1013 1014Objective-C Features 1015==================== 1016 1017Related result types 1018-------------------- 1019 1020According to Cocoa conventions, Objective-C methods with certain names 1021("``init``", "``alloc``", etc.) always return objects that are an instance of 1022the receiving class's type. Such methods are said to have a "related result 1023type", meaning that a message send to one of these methods will have the same 1024static type as an instance of the receiver class. For example, given the 1025following classes: 1026 1027.. code-block:: objc 1028 1029 @interface NSObject 1030 + (id)alloc; 1031 - (id)init; 1032 @end 1033 1034 @interface NSArray : NSObject 1035 @end 1036 1037and this common initialization pattern 1038 1039.. code-block:: objc 1040 1041 NSArray *array = [[NSArray alloc] init]; 1042 1043the type of the expression ``[NSArray alloc]`` is ``NSArray*`` because 1044``alloc`` implicitly has a related result type. Similarly, the type of the 1045expression ``[[NSArray alloc] init]`` is ``NSArray*``, since ``init`` has a 1046related result type and its receiver is known to have the type ``NSArray *``. 1047If neither ``alloc`` nor ``init`` had a related result type, the expressions 1048would have had type ``id``, as declared in the method signature. 1049 1050A method with a related result type can be declared by using the type 1051``instancetype`` as its result type. ``instancetype`` is a contextual keyword 1052that is only permitted in the result type of an Objective-C method, e.g. 1053 1054.. code-block:: objc 1055 1056 @interface A 1057 + (instancetype)constructAnA; 1058 @end 1059 1060The related result type can also be inferred for some methods. To determine 1061whether a method has an inferred related result type, the first word in the 1062camel-case selector (e.g., "``init``" in "``initWithObjects``") is considered, 1063and the method will have a related result type if its return type is compatible 1064with the type of its class and if: 1065 1066* the first word is "``alloc``" or "``new``", and the method is a class method, 1067 or 1068 1069* the first word is "``autorelease``", "``init``", "``retain``", or "``self``", 1070 and the method is an instance method. 1071 1072If a method with a related result type is overridden by a subclass method, the 1073subclass method must also return a type that is compatible with the subclass 1074type. For example: 1075 1076.. code-block:: objc 1077 1078 @interface NSString : NSObject 1079 - (NSUnrelated *)init; // incorrect usage: NSUnrelated is not NSString or a superclass of NSString 1080 @end 1081 1082Related result types only affect the type of a message send or property access 1083via the given method. In all other respects, a method with a related result 1084type is treated the same way as method that returns ``id``. 1085 1086Use ``__has_feature(objc_instancetype)`` to determine whether the 1087``instancetype`` contextual keyword is available. 1088 1089Automatic reference counting 1090---------------------------- 1091 1092Clang provides support for :doc:`automated reference counting 1093<AutomaticReferenceCounting>` in Objective-C, which eliminates the need 1094for manual ``retain``/``release``/``autorelease`` message sends. There are two 1095feature macros associated with automatic reference counting: 1096``__has_feature(objc_arc)`` indicates the availability of automated reference 1097counting in general, while ``__has_feature(objc_arc_weak)`` indicates that 1098automated reference counting also includes support for ``__weak`` pointers to 1099Objective-C objects. 1100 1101.. _objc-fixed-enum: 1102 1103Enumerations with a fixed underlying type 1104----------------------------------------- 1105 1106Clang provides support for C++11 enumerations with a fixed underlying type 1107within Objective-C. For example, one can write an enumeration type as: 1108 1109.. code-block:: c++ 1110 1111 typedef enum : unsigned char { Red, Green, Blue } Color; 1112 1113This specifies that the underlying type, which is used to store the enumeration 1114value, is ``unsigned char``. 1115 1116Use ``__has_feature(objc_fixed_enum)`` to determine whether support for fixed 1117underlying types is available in Objective-C. 1118 1119Interoperability with C++11 lambdas 1120----------------------------------- 1121 1122Clang provides interoperability between C++11 lambdas and blocks-based APIs, by 1123permitting a lambda to be implicitly converted to a block pointer with the 1124corresponding signature. For example, consider an API such as ``NSArray``'s 1125array-sorting method: 1126 1127.. code-block:: objc 1128 1129 - (NSArray *)sortedArrayUsingComparator:(NSComparator)cmptr; 1130 1131``NSComparator`` is simply a typedef for the block pointer ``NSComparisonResult 1132(^)(id, id)``, and parameters of this type are generally provided with block 1133literals as arguments. However, one can also use a C++11 lambda so long as it 1134provides the same signature (in this case, accepting two parameters of type 1135``id`` and returning an ``NSComparisonResult``): 1136 1137.. code-block:: objc 1138 1139 NSArray *array = @[@"string 1", @"string 21", @"string 12", @"String 11", 1140 @"String 02"]; 1141 const NSStringCompareOptions comparisonOptions 1142 = NSCaseInsensitiveSearch | NSNumericSearch | 1143 NSWidthInsensitiveSearch | NSForcedOrderingSearch; 1144 NSLocale *currentLocale = [NSLocale currentLocale]; 1145 NSArray *sorted 1146 = [array sortedArrayUsingComparator:[=](id s1, id s2) -> NSComparisonResult { 1147 NSRange string1Range = NSMakeRange(0, [s1 length]); 1148 return [s1 compare:s2 options:comparisonOptions 1149 range:string1Range locale:currentLocale]; 1150 }]; 1151 NSLog(@"sorted: %@", sorted); 1152 1153This code relies on an implicit conversion from the type of the lambda 1154expression (an unnamed, local class type called the *closure type*) to the 1155corresponding block pointer type. The conversion itself is expressed by a 1156conversion operator in that closure type that produces a block pointer with the 1157same signature as the lambda itself, e.g., 1158 1159.. code-block:: objc 1160 1161 operator NSComparisonResult (^)(id, id)() const; 1162 1163This conversion function returns a new block that simply forwards the two 1164parameters to the lambda object (which it captures by copy), then returns the 1165result. The returned block is first copied (with ``Block_copy``) and then 1166autoreleased. As an optimization, if a lambda expression is immediately 1167converted to a block pointer (as in the first example, above), then the block 1168is not copied and autoreleased: rather, it is given the same lifetime as a 1169block literal written at that point in the program, which avoids the overhead 1170of copying a block to the heap in the common case. 1171 1172The conversion from a lambda to a block pointer is only available in 1173Objective-C++, and not in C++ with blocks, due to its use of Objective-C memory 1174management (autorelease). 1175 1176Object Literals and Subscripting 1177-------------------------------- 1178 1179Clang provides support for :doc:`Object Literals and Subscripting 1180<ObjectiveCLiterals>` in Objective-C, which simplifies common Objective-C 1181programming patterns, makes programs more concise, and improves the safety of 1182container creation. There are several feature macros associated with object 1183literals and subscripting: ``__has_feature(objc_array_literals)`` tests the 1184availability of array literals; ``__has_feature(objc_dictionary_literals)`` 1185tests the availability of dictionary literals; 1186``__has_feature(objc_subscripting)`` tests the availability of object 1187subscripting. 1188 1189Objective-C Autosynthesis of Properties 1190--------------------------------------- 1191 1192Clang provides support for autosynthesis of declared properties. Using this 1193feature, clang provides default synthesis of those properties not declared 1194@dynamic and not having user provided backing getter and setter methods. 1195``__has_feature(objc_default_synthesize_properties)`` checks for availability 1196of this feature in version of clang being used. 1197 1198.. _langext-objc_method_family: 1199 1200 1201Objective-C requiring a call to ``super`` in an override 1202-------------------------------------------------------- 1203 1204Some Objective-C classes allow a subclass to override a particular method in a 1205parent class but expect that the overriding method also calls the overridden 1206method in the parent class. For these cases, we provide an attribute to 1207designate that a method requires a "call to ``super``" in the overriding 1208method in the subclass. 1209 1210**Usage**: ``__attribute__((objc_requires_super))``. This attribute can only 1211be placed at the end of a method declaration: 1212 1213.. code-block:: objc 1214 1215 - (void)foo __attribute__((objc_requires_super)); 1216 1217This attribute can only be applied the method declarations within a class, and 1218not a protocol. Currently this attribute does not enforce any placement of 1219where the call occurs in the overriding method (such as in the case of 1220``-dealloc`` where the call must appear at the end). It checks only that it 1221exists. 1222 1223Note that on both OS X and iOS that the Foundation framework provides a 1224convenience macro ``NS_REQUIRES_SUPER`` that provides syntactic sugar for this 1225attribute: 1226 1227.. code-block:: objc 1228 1229 - (void)foo NS_REQUIRES_SUPER; 1230 1231This macro is conditionally defined depending on the compiler's support for 1232this attribute. If the compiler does not support the attribute the macro 1233expands to nothing. 1234 1235Operationally, when a method has this annotation the compiler will warn if the 1236implementation of an override in a subclass does not call super. For example: 1237 1238.. code-block:: objc 1239 1240 warning: method possibly missing a [super AnnotMeth] call 1241 - (void) AnnotMeth{}; 1242 ^ 1243 1244Objective-C Method Families 1245--------------------------- 1246 1247Many methods in Objective-C have conventional meanings determined by their 1248selectors. It is sometimes useful to be able to mark a method as having a 1249particular conventional meaning despite not having the right selector, or as 1250not having the conventional meaning that its selector would suggest. For these 1251use cases, we provide an attribute to specifically describe the "method family" 1252that a method belongs to. 1253 1254**Usage**: ``__attribute__((objc_method_family(X)))``, where ``X`` is one of 1255``none``, ``alloc``, ``copy``, ``init``, ``mutableCopy``, or ``new``. This 1256attribute can only be placed at the end of a method declaration: 1257 1258.. code-block:: objc 1259 1260 - (NSString *)initMyStringValue __attribute__((objc_method_family(none))); 1261 1262Users who do not wish to change the conventional meaning of a method, and who 1263merely want to document its non-standard retain and release semantics, should 1264use the :ref:`retaining behavior attributes <langext-objc-retain-release>` 1265described below. 1266 1267Query for this feature with ``__has_attribute(objc_method_family)``. 1268 1269.. _langext-objc-retain-release: 1270 1271Objective-C retaining behavior attributes 1272----------------------------------------- 1273 1274In Objective-C, functions and methods are generally assumed to follow the 1275`Cocoa Memory Management 1276<http://developer.apple.com/library/mac/#documentation/Cocoa/Conceptual/MemoryMgmt/Articles/mmRules.html>`_ 1277conventions for ownership of object arguments and 1278return values. However, there are exceptions, and so Clang provides attributes 1279to allow these exceptions to be documented. This are used by ARC and the 1280`static analyzer <http://clang-analyzer.llvm.org>`_ Some exceptions may be 1281better described using the :ref:`objc_method_family 1282<langext-objc_method_family>` attribute instead. 1283 1284**Usage**: The ``ns_returns_retained``, ``ns_returns_not_retained``, 1285``ns_returns_autoreleased``, ``cf_returns_retained``, and 1286``cf_returns_not_retained`` attributes can be placed on methods and functions 1287that return Objective-C or CoreFoundation objects. They are commonly placed at 1288the end of a function prototype or method declaration: 1289 1290.. code-block:: objc 1291 1292 id foo() __attribute__((ns_returns_retained)); 1293 1294 - (NSString *)bar:(int)x __attribute__((ns_returns_retained)); 1295 1296The ``*_returns_retained`` attributes specify that the returned object has a +1 1297retain count. The ``*_returns_not_retained`` attributes specify that the return 1298object has a +0 retain count, even if the normal convention for its selector 1299would be +1. ``ns_returns_autoreleased`` specifies that the returned object is 1300+0, but is guaranteed to live at least as long as the next flush of an 1301autorelease pool. 1302 1303**Usage**: The ``ns_consumed`` and ``cf_consumed`` attributes can be placed on 1304an parameter declaration; they specify that the argument is expected to have a 1305+1 retain count, which will be balanced in some way by the function or method. 1306The ``ns_consumes_self`` attribute can only be placed on an Objective-C 1307method; it specifies that the method expects its ``self`` parameter to have a 1308+1 retain count, which it will balance in some way. 1309 1310.. code-block:: objc 1311 1312 void foo(__attribute__((ns_consumed)) NSString *string); 1313 1314 - (void) bar __attribute__((ns_consumes_self)); 1315 - (void) baz:(id) __attribute__((ns_consumed)) x; 1316 1317Further examples of these attributes are available in the static analyzer's `list of annotations for analysis 1318<http://clang-analyzer.llvm.org/annotations.html#cocoa_mem>`_. 1319 1320Query for these features with ``__has_attribute(ns_consumed)``, 1321``__has_attribute(ns_returns_retained)``, etc. 1322 1323 1324Objective-C++ ABI: protocol-qualifier mangling of parameters 1325------------------------------------------------------------ 1326 1327Starting with LLVM 3.4, Clang produces a new mangling for parameters whose 1328type is a qualified-``id`` (e.g., ``id<Foo>``). This mangling allows such 1329parameters to be differentiated from those with the regular unqualified ``id`` 1330type. 1331 1332This was a non-backward compatible mangling change to the ABI. This change 1333allows proper overloading, and also prevents mangling conflicts with template 1334parameters of protocol-qualified type. 1335 1336Query the presence of this new mangling with 1337``__has_feature(objc_protocol_qualifier_mangling)``. 1338 1339.. _langext-overloading: 1340 1341Function Overloading in C 1342========================= 1343 1344Clang provides support for C++ function overloading in C. Function overloading 1345in C is introduced using the ``overloadable`` attribute. For example, one 1346might provide several overloaded versions of a ``tgsin`` function that invokes 1347the appropriate standard function computing the sine of a value with ``float``, 1348``double``, or ``long double`` precision: 1349 1350.. code-block:: c 1351 1352 #include <math.h> 1353 float __attribute__((overloadable)) tgsin(float x) { return sinf(x); } 1354 double __attribute__((overloadable)) tgsin(double x) { return sin(x); } 1355 long double __attribute__((overloadable)) tgsin(long double x) { return sinl(x); } 1356 1357Given these declarations, one can call ``tgsin`` with a ``float`` value to 1358receive a ``float`` result, with a ``double`` to receive a ``double`` result, 1359etc. Function overloading in C follows the rules of C++ function overloading 1360to pick the best overload given the call arguments, with a few C-specific 1361semantics: 1362 1363* Conversion from ``float`` or ``double`` to ``long double`` is ranked as a 1364 floating-point promotion (per C99) rather than as a floating-point conversion 1365 (as in C++). 1366 1367* A conversion from a pointer of type ``T*`` to a pointer of type ``U*`` is 1368 considered a pointer conversion (with conversion rank) if ``T`` and ``U`` are 1369 compatible types. 1370 1371* A conversion from type ``T`` to a value of type ``U`` is permitted if ``T`` 1372 and ``U`` are compatible types. This conversion is given "conversion" rank. 1373 1374The declaration of ``overloadable`` functions is restricted to function 1375declarations and definitions. Most importantly, if any function with a given 1376name is given the ``overloadable`` attribute, then all function declarations 1377and definitions with that name (and in that scope) must have the 1378``overloadable`` attribute. This rule even applies to redeclarations of 1379functions whose original declaration had the ``overloadable`` attribute, e.g., 1380 1381.. code-block:: c 1382 1383 int f(int) __attribute__((overloadable)); 1384 float f(float); // error: declaration of "f" must have the "overloadable" attribute 1385 1386 int g(int) __attribute__((overloadable)); 1387 int g(int) { } // error: redeclaration of "g" must also have the "overloadable" attribute 1388 1389Functions marked ``overloadable`` must have prototypes. Therefore, the 1390following code is ill-formed: 1391 1392.. code-block:: c 1393 1394 int h() __attribute__((overloadable)); // error: h does not have a prototype 1395 1396However, ``overloadable`` functions are allowed to use a ellipsis even if there 1397are no named parameters (as is permitted in C++). This feature is particularly 1398useful when combined with the ``unavailable`` attribute: 1399 1400.. code-block:: c++ 1401 1402 void honeypot(...) __attribute__((overloadable, unavailable)); // calling me is an error 1403 1404Functions declared with the ``overloadable`` attribute have their names mangled 1405according to the same rules as C++ function names. For example, the three 1406``tgsin`` functions in our motivating example get the mangled names 1407``_Z5tgsinf``, ``_Z5tgsind``, and ``_Z5tgsine``, respectively. There are two 1408caveats to this use of name mangling: 1409 1410* Future versions of Clang may change the name mangling of functions overloaded 1411 in C, so you should not depend on an specific mangling. To be completely 1412 safe, we strongly urge the use of ``static inline`` with ``overloadable`` 1413 functions. 1414 1415* The ``overloadable`` attribute has almost no meaning when used in C++, 1416 because names will already be mangled and functions are already overloadable. 1417 However, when an ``overloadable`` function occurs within an ``extern "C"`` 1418 linkage specification, it's name *will* be mangled in the same way as it 1419 would in C. 1420 1421Query for this feature with ``__has_extension(attribute_overloadable)``. 1422 1423Controlling Overload Resolution 1424=============================== 1425 1426Clang introduces the ``enable_if`` attribute, which can be placed on function 1427declarations to control which overload is selected based on the values of the 1428function's arguments. When combined with the 1429:ref:`overloadable<langext-overloading>` attribute, this feature is also 1430available in C. 1431 1432.. code-block:: c++ 1433 1434 int isdigit(int c); 1435 int isdigit(int c) __attribute__((enable_if(c <= -1 || c > 255, "chosen when 'c' is out of range"))) __attribute__((unavailable("'c' must have the value of an unsigned char or EOF"))); 1436 1437 void foo(char c) { 1438 isdigit(c); 1439 isdigit(10); 1440 isdigit(-10); // results in a compile-time error. 1441 } 1442 1443The enable_if attribute takes two arguments, the first is an expression written 1444in terms of the function parameters, the second is a string explaining why this 1445overload candidate could not be selected to be displayed in diagnostics. The 1446expression is part of the function signature for the purposes of determining 1447whether it is a redeclaration (following the rules used when determining 1448whether a C++ template specialization is ODR-equivalent), but is not part of 1449the type. 1450 1451The enable_if expression is evaluated as if it were the body of a 1452bool-returning constexpr function declared with the arguments of the function 1453it is being applied to, then called with the parameters at the callsite. If the 1454result is false or could not be determined through constant expression 1455evaluation, then this overload will not be chosen and the provided string may 1456be used in a diagnostic if the compile fails as a result. 1457 1458Because the enable_if expression is an unevaluated context, there are no global 1459state changes, nor the ability to pass information from the enable_if 1460expression to the function body. For example, suppose we want calls to 1461strnlen(strbuf, maxlen) to resolve to strnlen_chk(strbuf, maxlen, size of 1462strbuf) only if the size of strbuf can be determined: 1463 1464.. code-block:: c++ 1465 1466 __attribute__((always_inline)) 1467 static inline size_t strnlen(const char *s, size_t maxlen) 1468 __attribute__((overloadable)) 1469 __attribute__((enable_if(__builtin_object_size(s, 0) != -1))), 1470 "chosen when the buffer size is known but 'maxlen' is not"))) 1471 { 1472 return strnlen_chk(s, maxlen, __builtin_object_size(s, 0)); 1473 } 1474 1475Multiple enable_if attributes may be applied to a single declaration. In this 1476case, the enable_if expressions are evaluated from left to right in the 1477following manner. First, the candidates whose enable_if expressions evaluate to 1478false or cannot be evaluated are discarded. If the remaining candidates do not 1479share ODR-equivalent enable_if expressions, the overload resolution is 1480ambiguous. Otherwise, enable_if overload resolution continues with the next 1481enable_if attribute on the candidates that have not been discarded and have 1482remaining enable_if attributes. In this way, we pick the most specific 1483overload out of a number of viable overloads using enable_if. 1484 1485.. code-block:: c++ 1486 1487 void f() __attribute__((enable_if(true, ""))); // #1 1488 void f() __attribute__((enable_if(true, ""))) __attribute__((enable_if(true, ""))); // #2 1489 1490 void g(int i, int j) __attribute__((enable_if(i, ""))); // #1 1491 void g(int i, int j) __attribute__((enable_if(j, ""))) __attribute__((enable_if(true))); // #2 1492 1493In this example, a call to f() is always resolved to #2, as the first enable_if 1494expression is ODR-equivalent for both declarations, but #1 does not have another 1495enable_if expression to continue evaluating, so the next round of evaluation has 1496only a single candidate. In a call to g(1, 1), the call is ambiguous even though 1497#2 has more enable_if attributes, because the first enable_if expressions are 1498not ODR-equivalent. 1499 1500Query for this feature with ``__has_attribute(enable_if)``. 1501 1502Initializer lists for complex numbers in C 1503========================================== 1504 1505clang supports an extension which allows the following in C: 1506 1507.. code-block:: c++ 1508 1509 #include <math.h> 1510 #include <complex.h> 1511 complex float x = { 1.0f, INFINITY }; // Init to (1, Inf) 1512 1513This construct is useful because there is no way to separately initialize the 1514real and imaginary parts of a complex variable in standard C, given that clang 1515does not support ``_Imaginary``. (Clang also supports the ``__real__`` and 1516``__imag__`` extensions from gcc, which help in some cases, but are not usable 1517in static initializers.) 1518 1519Note that this extension does not allow eliding the braces; the meaning of the 1520following two lines is different: 1521 1522.. code-block:: c++ 1523 1524 complex float x[] = { { 1.0f, 1.0f } }; // [0] = (1, 1) 1525 complex float x[] = { 1.0f, 1.0f }; // [0] = (1, 0), [1] = (1, 0) 1526 1527This extension also works in C++ mode, as far as that goes, but does not apply 1528to the C++ ``std::complex``. (In C++11, list initialization allows the same 1529syntax to be used with ``std::complex`` with the same meaning.) 1530 1531Builtin Functions 1532================= 1533 1534Clang supports a number of builtin library functions with the same syntax as 1535GCC, including things like ``__builtin_nan``, ``__builtin_constant_p``, 1536``__builtin_choose_expr``, ``__builtin_types_compatible_p``, 1537``__sync_fetch_and_add``, etc. In addition to the GCC builtins, Clang supports 1538a number of builtins that GCC does not, which are listed here. 1539 1540Please note that Clang does not and will not support all of the GCC builtins 1541for vector operations. Instead of using builtins, you should use the functions 1542defined in target-specific header files like ``<xmmintrin.h>``, which define 1543portable wrappers for these. Many of the Clang versions of these functions are 1544implemented directly in terms of :ref:`extended vector support 1545<langext-vectors>` instead of builtins, in order to reduce the number of 1546builtins that we need to implement. 1547 1548``__builtin_readcyclecounter`` 1549------------------------------ 1550 1551``__builtin_readcyclecounter`` is used to access the cycle counter register (or 1552a similar low-latency, high-accuracy clock) on those targets that support it. 1553 1554**Syntax**: 1555 1556.. code-block:: c++ 1557 1558 __builtin_readcyclecounter() 1559 1560**Example of Use**: 1561 1562.. code-block:: c++ 1563 1564 unsigned long long t0 = __builtin_readcyclecounter(); 1565 do_something(); 1566 unsigned long long t1 = __builtin_readcyclecounter(); 1567 unsigned long long cycles_to_do_something = t1 - t0; // assuming no overflow 1568 1569**Description**: 1570 1571The ``__builtin_readcyclecounter()`` builtin returns the cycle counter value, 1572which may be either global or process/thread-specific depending on the target. 1573As the backing counters often overflow quickly (on the order of seconds) this 1574should only be used for timing small intervals. When not supported by the 1575target, the return value is always zero. This builtin takes no arguments and 1576produces an unsigned long long result. 1577 1578Query for this feature with ``__has_builtin(__builtin_readcyclecounter)``. Note 1579that even if present, its use may depend on run-time privilege or other OS 1580controlled state. 1581 1582.. _langext-__builtin_shufflevector: 1583 1584``__builtin_shufflevector`` 1585--------------------------- 1586 1587``__builtin_shufflevector`` is used to express generic vector 1588permutation/shuffle/swizzle operations. This builtin is also very important 1589for the implementation of various target-specific header files like 1590``<xmmintrin.h>``. 1591 1592**Syntax**: 1593 1594.. code-block:: c++ 1595 1596 __builtin_shufflevector(vec1, vec2, index1, index2, ...) 1597 1598**Examples**: 1599 1600.. code-block:: c++ 1601 1602 // identity operation - return 4-element vector v1. 1603 __builtin_shufflevector(v1, v1, 0, 1, 2, 3) 1604 1605 // "Splat" element 0 of V1 into a 4-element result. 1606 __builtin_shufflevector(V1, V1, 0, 0, 0, 0) 1607 1608 // Reverse 4-element vector V1. 1609 __builtin_shufflevector(V1, V1, 3, 2, 1, 0) 1610 1611 // Concatenate every other element of 4-element vectors V1 and V2. 1612 __builtin_shufflevector(V1, V2, 0, 2, 4, 6) 1613 1614 // Concatenate every other element of 8-element vectors V1 and V2. 1615 __builtin_shufflevector(V1, V2, 0, 2, 4, 6, 8, 10, 12, 14) 1616 1617 // Shuffle v1 with some elements being undefined 1618 __builtin_shufflevector(v1, v1, 3, -1, 1, -1) 1619 1620**Description**: 1621 1622The first two arguments to ``__builtin_shufflevector`` are vectors that have 1623the same element type. The remaining arguments are a list of integers that 1624specify the elements indices of the first two vectors that should be extracted 1625and returned in a new vector. These element indices are numbered sequentially 1626starting with the first vector, continuing into the second vector. Thus, if 1627``vec1`` is a 4-element vector, index 5 would refer to the second element of 1628``vec2``. An index of -1 can be used to indicate that the corresponding element 1629in the returned vector is a don't care and can be optimized by the backend. 1630 1631The result of ``__builtin_shufflevector`` is a vector with the same element 1632type as ``vec1``/``vec2`` but that has an element count equal to the number of 1633indices specified. 1634 1635Query for this feature with ``__has_builtin(__builtin_shufflevector)``. 1636 1637``__builtin_convertvector`` 1638--------------------------- 1639 1640``__builtin_convertvector`` is used to express generic vector 1641type-conversion operations. The input vector and the output vector 1642type must have the same number of elements. 1643 1644**Syntax**: 1645 1646.. code-block:: c++ 1647 1648 __builtin_convertvector(src_vec, dst_vec_type) 1649 1650**Examples**: 1651 1652.. code-block:: c++ 1653 1654 typedef double vector4double __attribute__((__vector_size__(32))); 1655 typedef float vector4float __attribute__((__vector_size__(16))); 1656 typedef short vector4short __attribute__((__vector_size__(8))); 1657 vector4float vf; vector4short vs; 1658 1659 // convert from a vector of 4 floats to a vector of 4 doubles. 1660 __builtin_convertvector(vf, vector4double) 1661 // equivalent to: 1662 (vector4double) { (double) vf[0], (double) vf[1], (double) vf[2], (double) vf[3] } 1663 1664 // convert from a vector of 4 shorts to a vector of 4 floats. 1665 __builtin_convertvector(vs, vector4float) 1666 // equivalent to: 1667 (vector4float) { (float) vf[0], (float) vf[1], (float) vf[2], (float) vf[3] } 1668 1669**Description**: 1670 1671The first argument to ``__builtin_convertvector`` is a vector, and the second 1672argument is a vector type with the same number of elements as the first 1673argument. 1674 1675The result of ``__builtin_convertvector`` is a vector with the same element 1676type as the second argument, with a value defined in terms of the action of a 1677C-style cast applied to each element of the first argument. 1678 1679Query for this feature with ``__has_builtin(__builtin_convertvector)``. 1680 1681``__builtin_unreachable`` 1682------------------------- 1683 1684``__builtin_unreachable`` is used to indicate that a specific point in the 1685program cannot be reached, even if the compiler might otherwise think it can. 1686This is useful to improve optimization and eliminates certain warnings. For 1687example, without the ``__builtin_unreachable`` in the example below, the 1688compiler assumes that the inline asm can fall through and prints a "function 1689declared '``noreturn``' should not return" warning. 1690 1691**Syntax**: 1692 1693.. code-block:: c++ 1694 1695 __builtin_unreachable() 1696 1697**Example of use**: 1698 1699.. code-block:: c++ 1700 1701 void myabort(void) __attribute__((noreturn)); 1702 void myabort(void) { 1703 asm("int3"); 1704 __builtin_unreachable(); 1705 } 1706 1707**Description**: 1708 1709The ``__builtin_unreachable()`` builtin has completely undefined behavior. 1710Since it has undefined behavior, it is a statement that it is never reached and 1711the optimizer can take advantage of this to produce better code. This builtin 1712takes no arguments and produces a void result. 1713 1714Query for this feature with ``__has_builtin(__builtin_unreachable)``. 1715 1716``__sync_swap`` 1717--------------- 1718 1719``__sync_swap`` is used to atomically swap integers or pointers in memory. 1720 1721**Syntax**: 1722 1723.. code-block:: c++ 1724 1725 type __sync_swap(type *ptr, type value, ...) 1726 1727**Example of Use**: 1728 1729.. code-block:: c++ 1730 1731 int old_value = __sync_swap(&value, new_value); 1732 1733**Description**: 1734 1735The ``__sync_swap()`` builtin extends the existing ``__sync_*()`` family of 1736atomic intrinsics to allow code to atomically swap the current value with the 1737new value. More importantly, it helps developers write more efficient and 1738correct code by avoiding expensive loops around 1739``__sync_bool_compare_and_swap()`` or relying on the platform specific 1740implementation details of ``__sync_lock_test_and_set()``. The 1741``__sync_swap()`` builtin is a full barrier. 1742 1743``__builtin_addressof`` 1744----------------------- 1745 1746``__builtin_addressof`` performs the functionality of the built-in ``&`` 1747operator, ignoring any ``operator&`` overload. This is useful in constant 1748expressions in C++11, where there is no other way to take the address of an 1749object that overloads ``operator&``. 1750 1751**Example of use**: 1752 1753.. code-block:: c++ 1754 1755 template<typename T> constexpr T *addressof(T &value) { 1756 return __builtin_addressof(value); 1757 } 1758 1759Multiprecision Arithmetic Builtins 1760---------------------------------- 1761 1762Clang provides a set of builtins which expose multiprecision arithmetic in a 1763manner amenable to C. They all have the following form: 1764 1765.. code-block:: c 1766 1767 unsigned x = ..., y = ..., carryin = ..., carryout; 1768 unsigned sum = __builtin_addc(x, y, carryin, &carryout); 1769 1770Thus one can form a multiprecision addition chain in the following manner: 1771 1772.. code-block:: c 1773 1774 unsigned *x, *y, *z, carryin=0, carryout; 1775 z[0] = __builtin_addc(x[0], y[0], carryin, &carryout); 1776 carryin = carryout; 1777 z[1] = __builtin_addc(x[1], y[1], carryin, &carryout); 1778 carryin = carryout; 1779 z[2] = __builtin_addc(x[2], y[2], carryin, &carryout); 1780 carryin = carryout; 1781 z[3] = __builtin_addc(x[3], y[3], carryin, &carryout); 1782 1783The complete list of builtins are: 1784 1785.. code-block:: c 1786 1787 unsigned char __builtin_addcb (unsigned char x, unsigned char y, unsigned char carryin, unsigned char *carryout); 1788 unsigned short __builtin_addcs (unsigned short x, unsigned short y, unsigned short carryin, unsigned short *carryout); 1789 unsigned __builtin_addc (unsigned x, unsigned y, unsigned carryin, unsigned *carryout); 1790 unsigned long __builtin_addcl (unsigned long x, unsigned long y, unsigned long carryin, unsigned long *carryout); 1791 unsigned long long __builtin_addcll(unsigned long long x, unsigned long long y, unsigned long long carryin, unsigned long long *carryout); 1792 unsigned char __builtin_subcb (unsigned char x, unsigned char y, unsigned char carryin, unsigned char *carryout); 1793 unsigned short __builtin_subcs (unsigned short x, unsigned short y, unsigned short carryin, unsigned short *carryout); 1794 unsigned __builtin_subc (unsigned x, unsigned y, unsigned carryin, unsigned *carryout); 1795 unsigned long __builtin_subcl (unsigned long x, unsigned long y, unsigned long carryin, unsigned long *carryout); 1796 unsigned long long __builtin_subcll(unsigned long long x, unsigned long long y, unsigned long long carryin, unsigned long long *carryout); 1797 1798Checked Arithmetic Builtins 1799--------------------------- 1800 1801Clang provides a set of builtins that implement checked arithmetic for security 1802critical applications in a manner that is fast and easily expressable in C. As 1803an example of their usage: 1804 1805.. code-block:: c 1806 1807 errorcode_t security_critical_application(...) { 1808 unsigned x, y, result; 1809 ... 1810 if (__builtin_umul_overflow(x, y, &result)) 1811 return kErrorCodeHackers; 1812 ... 1813 use_multiply(result); 1814 ... 1815 } 1816 1817A complete enumeration of the builtins are: 1818 1819.. code-block:: c 1820 1821 bool __builtin_uadd_overflow (unsigned x, unsigned y, unsigned *sum); 1822 bool __builtin_uaddl_overflow (unsigned long x, unsigned long y, unsigned long *sum); 1823 bool __builtin_uaddll_overflow(unsigned long long x, unsigned long long y, unsigned long long *sum); 1824 bool __builtin_usub_overflow (unsigned x, unsigned y, unsigned *diff); 1825 bool __builtin_usubl_overflow (unsigned long x, unsigned long y, unsigned long *diff); 1826 bool __builtin_usubll_overflow(unsigned long long x, unsigned long long y, unsigned long long *diff); 1827 bool __builtin_umul_overflow (unsigned x, unsigned y, unsigned *prod); 1828 bool __builtin_umull_overflow (unsigned long x, unsigned long y, unsigned long *prod); 1829 bool __builtin_umulll_overflow(unsigned long long x, unsigned long long y, unsigned long long *prod); 1830 bool __builtin_sadd_overflow (int x, int y, int *sum); 1831 bool __builtin_saddl_overflow (long x, long y, long *sum); 1832 bool __builtin_saddll_overflow(long long x, long long y, long long *sum); 1833 bool __builtin_ssub_overflow (int x, int y, int *diff); 1834 bool __builtin_ssubl_overflow (long x, long y, long *diff); 1835 bool __builtin_ssubll_overflow(long long x, long long y, long long *diff); 1836 bool __builtin_smul_overflow (int x, int y, int *prod); 1837 bool __builtin_smull_overflow (long x, long y, long *prod); 1838 bool __builtin_smulll_overflow(long long x, long long y, long long *prod); 1839 1840 1841.. _langext-__c11_atomic: 1842 1843__c11_atomic builtins 1844--------------------- 1845 1846Clang provides a set of builtins which are intended to be used to implement 1847C11's ``<stdatomic.h>`` header. These builtins provide the semantics of the 1848``_explicit`` form of the corresponding C11 operation, and are named with a 1849``__c11_`` prefix. The supported operations are: 1850 1851* ``__c11_atomic_init`` 1852* ``__c11_atomic_thread_fence`` 1853* ``__c11_atomic_signal_fence`` 1854* ``__c11_atomic_is_lock_free`` 1855* ``__c11_atomic_store`` 1856* ``__c11_atomic_load`` 1857* ``__c11_atomic_exchange`` 1858* ``__c11_atomic_compare_exchange_strong`` 1859* ``__c11_atomic_compare_exchange_weak`` 1860* ``__c11_atomic_fetch_add`` 1861* ``__c11_atomic_fetch_sub`` 1862* ``__c11_atomic_fetch_and`` 1863* ``__c11_atomic_fetch_or`` 1864* ``__c11_atomic_fetch_xor`` 1865 1866Low-level ARM exclusive memory builtins 1867--------------------------------------- 1868 1869Clang provides overloaded builtins giving direct access to the three key ARM 1870instructions for implementing atomic operations. 1871 1872.. code-block:: c 1873 1874 T __builtin_arm_ldrex(const volatile T *addr); 1875 int __builtin_arm_strex(T val, volatile T *addr); 1876 void __builtin_arm_clrex(void); 1877 1878The types ``T`` currently supported are: 1879* Integer types with width at most 64 bits. 1880* Floating-point types 1881* Pointer types. 1882 1883Note that the compiler does not guarantee it will not insert stores which clear 1884the exclusive monitor in between an ``ldrex`` and its paired ``strex``. In 1885practice this is only usually a risk when the extra store is on the same cache 1886line as the variable being modified and Clang will only insert stack stores on 1887its own, so it is best not to use these operations on variables with automatic 1888storage duration. 1889 1890Also, loads and stores may be implicit in code written between the ``ldrex`` and 1891``strex``. Clang will not necessarily mitigate the effects of these either, so 1892care should be exercised. 1893 1894For these reasons the higher level atomic primitives should be preferred where 1895possible. 1896 1897Non-standard C++11 Attributes 1898============================= 1899 1900Clang's non-standard C++11 attributes live in the ``clang`` attribute 1901namespace. 1902 1903The ``clang::fallthrough`` attribute 1904------------------------------------ 1905 1906The ``clang::fallthrough`` attribute is used along with the 1907``-Wimplicit-fallthrough`` argument to annotate intentional fall-through 1908between switch labels. It can only be applied to a null statement placed at a 1909point of execution between any statement and the next switch label. It is 1910common to mark these places with a specific comment, but this attribute is 1911meant to replace comments with a more strict annotation, which can be checked 1912by the compiler. This attribute doesn't change semantics of the code and can 1913be used wherever an intended fall-through occurs. It is designed to mimic 1914control-flow statements like ``break;``, so it can be placed in most places 1915where ``break;`` can, but only if there are no statements on the execution path 1916between it and the next switch label. 1917 1918Here is an example: 1919 1920.. code-block:: c++ 1921 1922 // compile with -Wimplicit-fallthrough 1923 switch (n) { 1924 case 22: 1925 case 33: // no warning: no statements between case labels 1926 f(); 1927 case 44: // warning: unannotated fall-through 1928 g(); 1929 [[clang::fallthrough]]; 1930 case 55: // no warning 1931 if (x) { 1932 h(); 1933 break; 1934 } 1935 else { 1936 i(); 1937 [[clang::fallthrough]]; 1938 } 1939 case 66: // no warning 1940 p(); 1941 [[clang::fallthrough]]; // warning: fallthrough annotation does not 1942 // directly precede case label 1943 q(); 1944 case 77: // warning: unannotated fall-through 1945 r(); 1946 } 1947 1948``gnu::`` attributes 1949-------------------- 1950 1951Clang also supports GCC's ``gnu`` attribute namespace. All GCC attributes which 1952are accepted with the ``__attribute__((foo))`` syntax are also accepted as 1953``[[gnu::foo]]``. This only extends to attributes which are specified by GCC 1954(see the list of `GCC function attributes 1955<http://gcc.gnu.org/onlinedocs/gcc/Function-Attributes.html>`_, `GCC variable 1956attributes <http://gcc.gnu.org/onlinedocs/gcc/Variable-Attributes.html>`_, and 1957`GCC type attributes 1958<http://gcc.gnu.org/onlinedocs/gcc/Type-Attributes.html>`_). As with the GCC 1959implementation, these attributes must appertain to the *declarator-id* in a 1960declaration, which means they must go either at the start of the declaration or 1961immediately after the name being declared. 1962 1963For example, this applies the GNU ``unused`` attribute to ``a`` and ``f``, and 1964also applies the GNU ``noreturn`` attribute to ``f``. 1965 1966.. code-block:: c++ 1967 1968 [[gnu::unused]] int a, f [[gnu::noreturn]] (); 1969 1970Target-Specific Extensions 1971========================== 1972 1973Clang supports some language features conditionally on some targets. 1974 1975X86/X86-64 Language Extensions 1976------------------------------ 1977 1978The X86 backend has these language extensions: 1979 1980Memory references off the GS segment 1981^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ 1982 1983Annotating a pointer with address space #256 causes it to be code generated 1984relative to the X86 GS segment register, and address space #257 causes it to be 1985relative to the X86 FS segment. Note that this is a very very low-level 1986feature that should only be used if you know what you're doing (for example in 1987an OS kernel). 1988 1989Here is an example: 1990 1991.. code-block:: c++ 1992 1993 #define GS_RELATIVE __attribute__((address_space(256))) 1994 int foo(int GS_RELATIVE *P) { 1995 return *P; 1996 } 1997 1998Which compiles to (on X86-32): 1999 2000.. code-block:: gas 2001 2002 _foo: 2003 movl 4(%esp), %eax 2004 movl %gs:(%eax), %eax 2005 ret 2006 2007ARM Language Extensions 2008----------------------- 2009 2010Interrupt attribute 2011^^^^^^^^^^^^^^^^^^^ 2012 2013Clang supports the GNU style ``__attribute__((interrupt("TYPE")))`` attribute on 2014ARM targets. This attribute may be attached to a function definition and 2015instructs the backend to generate appropriate function entry/exit code so that 2016it can be used directly as an interrupt service routine. 2017 2018The parameter passed to the interrupt attribute is optional, but if 2019provided it must be a string literal with one of the following values: "IRQ", 2020"FIQ", "SWI", "ABORT", "UNDEF". 2021 2022The semantics are as follows: 2023 2024- If the function is AAPCS, Clang instructs the backend to realign the stack to 2025 8 bytes on entry. This is a general requirement of the AAPCS at public 2026 interfaces, but may not hold when an exception is taken. Doing this allows 2027 other AAPCS functions to be called. 2028- If the CPU is M-class this is all that needs to be done since the architecture 2029 itself is designed in such a way that functions obeying the normal AAPCS ABI 2030 constraints are valid exception handlers. 2031- If the CPU is not M-class, the prologue and epilogue are modified to save all 2032 non-banked registers that are used, so that upon return the user-mode state 2033 will not be corrupted. Note that to avoid unnecessary overhead, only 2034 general-purpose (integer) registers are saved in this way. If VFP operations 2035 are needed, that state must be saved manually. 2036 2037 Specifically, interrupt kinds other than "FIQ" will save all core registers 2038 except "lr" and "sp". "FIQ" interrupts will save r0-r7. 2039- If the CPU is not M-class, the return instruction is changed to one of the 2040 canonical sequences permitted by the architecture for exception return. Where 2041 possible the function itself will make the necessary "lr" adjustments so that 2042 the "preferred return address" is selected. 2043 2044 Unfortunately the compiler is unable to make this guarantee for an "UNDEF" 2045 handler, where the offset from "lr" to the preferred return address depends on 2046 the execution state of the code which generated the exception. In this case 2047 a sequence equivalent to "movs pc, lr" will be used. 2048 2049Extensions for Static Analysis 2050============================== 2051 2052Clang supports additional attributes that are useful for documenting program 2053invariants and rules for static analysis tools, such as the `Clang Static 2054Analyzer <http://clang-analyzer.llvm.org/>`_. These attributes are documented 2055in the analyzer's `list of source-level annotations 2056<http://clang-analyzer.llvm.org/annotations.html>`_. 2057 2058 2059Extensions for Dynamic Analysis 2060=============================== 2061 2062.. _langext-address_sanitizer: 2063 2064AddressSanitizer 2065---------------- 2066 2067Use ``__has_feature(address_sanitizer)`` to check if the code is being built 2068with :doc:`AddressSanitizer`. 2069 2070Use ``__attribute__((no_sanitize_address))`` 2071on a function declaration 2072to specify that address safety instrumentation (e.g. AddressSanitizer) should 2073not be applied to that function. 2074 2075.. _langext-thread_sanitizer: 2076 2077ThreadSanitizer 2078---------------- 2079 2080Use ``__has_feature(thread_sanitizer)`` to check if the code is being built 2081with :doc:`ThreadSanitizer`. 2082 2083Use ``__attribute__((no_sanitize_thread))`` on a function declaration 2084to specify that checks for data races on plain (non-atomic) memory accesses 2085should not be inserted by ThreadSanitizer. 2086The function is still instrumented by the tool to avoid false positives and 2087provide meaningful stack traces. 2088 2089.. _langext-memory_sanitizer: 2090 2091MemorySanitizer 2092---------------- 2093Use ``__has_feature(memory_sanitizer)`` to check if the code is being built 2094with :doc:`MemorySanitizer`. 2095 2096Use ``__attribute__((no_sanitize_memory))`` on a function declaration 2097to specify that checks for uninitialized memory should not be inserted 2098(e.g. by MemorySanitizer). The function may still be instrumented by the tool 2099to avoid false positives in other places. 2100 2101 2102Thread Safety Analysis 2103====================== 2104 2105Clang Thread Safety Analysis is a C++ language extension which warns about 2106potential race conditions in code. The analysis works very much like a type 2107system for multi-threaded programs. In addition to declaring the *type* of 2108data (e.g. ``int``, ``float``, etc.), the programmer can (optionally) declare 2109how access to that data is controlled in a multi-threaded environment. The 2110compiler will then issue warnings whenever code fails to follow obey the 2111declared requirements. 2112 2113The complete list of thread safety attributes, along with examples and 2114frequently asked questions, can be found in the main documentation: see 2115:doc:`ThreadSafetyAnalysis`. 2116 2117 2118Consumed Annotation Checking 2119============================ 2120 2121Clang supports additional attributes for checking basic resource management 2122properties, specifically for unique objects that have a single owning reference. 2123The following attributes are currently supported, although **the implementation 2124for these annotations is currently in development and are subject to change.** 2125 2126``consumable`` 2127-------------- 2128 2129Each class that uses any of the following annotations must first be marked 2130using the consumable attribute. Failure to do so will result in a warning. 2131 2132``set_typestate(new_state)`` 2133---------------------------- 2134 2135Annotate methods that transition an object into a new state with 2136``__attribute__((set_typestate(new_state)))``. The new new state must be 2137unconsumed, consumed, or unknown. 2138 2139``callable_when(...)`` 2140---------------------- 2141 2142Use ``__attribute__((callable_when(...)))`` to indicate what states a method 2143may be called in. Valid states are unconsumed, consumed, or unknown. Each 2144argument to this attribute must be a quoted string. E.g.: 2145 2146``__attribute__((callable_when("unconsumed", "unknown")))`` 2147 2148``tests_typestate(tested_state)`` 2149--------------------------------- 2150 2151Use ``__attribute__((tests_typestate(tested_state)))`` to indicate that a method 2152returns true if the object is in the specified state.. 2153 2154``param_typestate(expected_state)`` 2155----------------------------------- 2156 2157This attribute specifies expectations about function parameters. Calls to an 2158function with annotated parameters will issue a warning if the corresponding 2159argument isn't in the expected state. The attribute is also used to set the 2160initial state of the parameter when analyzing the function's body. 2161 2162``return_typestate(ret_state)`` 2163------------------------------- 2164 2165The ``return_typestate`` attribute can be applied to functions or parameters. 2166When applied to a function the attribute specifies the state of the returned 2167value. The function's body is checked to ensure that it always returns a value 2168in the specified state. On the caller side, values returned by the annotated 2169function are initialized to the given state. 2170 2171If the attribute is applied to a function parameter it modifies the state of 2172an argument after a call to the function returns. The function's body is 2173checked to ensure that the parameter is in the expected state before returning. 2174 2175Type Safety Checking 2176==================== 2177 2178Clang supports additional attributes to enable checking type safety properties 2179that can't be enforced by the C type system. Use cases include: 2180 2181* MPI library implementations, where these attributes enable checking that 2182 the buffer type matches the passed ``MPI_Datatype``; 2183* for HDF5 library there is a similar use case to MPI; 2184* checking types of variadic functions' arguments for functions like 2185 ``fcntl()`` and ``ioctl()``. 2186 2187You can detect support for these attributes with ``__has_attribute()``. For 2188example: 2189 2190.. code-block:: c++ 2191 2192 #if defined(__has_attribute) 2193 # if __has_attribute(argument_with_type_tag) && \ 2194 __has_attribute(pointer_with_type_tag) && \ 2195 __has_attribute(type_tag_for_datatype) 2196 # define ATTR_MPI_PWT(buffer_idx, type_idx) __attribute__((pointer_with_type_tag(mpi,buffer_idx,type_idx))) 2197 /* ... other macros ... */ 2198 # endif 2199 #endif 2200 2201 #if !defined(ATTR_MPI_PWT) 2202 # define ATTR_MPI_PWT(buffer_idx, type_idx) 2203 #endif 2204 2205 int MPI_Send(void *buf, int count, MPI_Datatype datatype /*, other args omitted */) 2206 ATTR_MPI_PWT(1,3); 2207 2208``argument_with_type_tag(...)`` 2209------------------------------- 2210 2211Use ``__attribute__((argument_with_type_tag(arg_kind, arg_idx, 2212type_tag_idx)))`` on a function declaration to specify that the function 2213accepts a type tag that determines the type of some other argument. 2214``arg_kind`` is an identifier that should be used when annotating all 2215applicable type tags. 2216 2217This attribute is primarily useful for checking arguments of variadic functions 2218(``pointer_with_type_tag`` can be used in most non-variadic cases). 2219 2220For example: 2221 2222.. code-block:: c++ 2223 2224 int fcntl(int fd, int cmd, ...) 2225 __attribute__(( argument_with_type_tag(fcntl,3,2) )); 2226 2227``pointer_with_type_tag(...)`` 2228------------------------------ 2229 2230Use ``__attribute__((pointer_with_type_tag(ptr_kind, ptr_idx, type_tag_idx)))`` 2231on a function declaration to specify that the function accepts a type tag that 2232determines the pointee type of some other pointer argument. 2233 2234For example: 2235 2236.. code-block:: c++ 2237 2238 int MPI_Send(void *buf, int count, MPI_Datatype datatype /*, other args omitted */) 2239 __attribute__(( pointer_with_type_tag(mpi,1,3) )); 2240 2241``type_tag_for_datatype(...)`` 2242------------------------------ 2243 2244Clang supports annotating type tags of two forms. 2245 2246* **Type tag that is an expression containing a reference to some declared 2247 identifier.** Use ``__attribute__((type_tag_for_datatype(kind, type)))`` on a 2248 declaration with that identifier: 2249 2250 .. code-block:: c++ 2251 2252 extern struct mpi_datatype mpi_datatype_int 2253 __attribute__(( type_tag_for_datatype(mpi,int) )); 2254 #define MPI_INT ((MPI_Datatype) &mpi_datatype_int) 2255 2256* **Type tag that is an integral literal.** Introduce a ``static const`` 2257 variable with a corresponding initializer value and attach 2258 ``__attribute__((type_tag_for_datatype(kind, type)))`` on that declaration, 2259 for example: 2260 2261 .. code-block:: c++ 2262 2263 #define MPI_INT ((MPI_Datatype) 42) 2264 static const MPI_Datatype mpi_datatype_int 2265 __attribute__(( type_tag_for_datatype(mpi,int) )) = 42 2266 2267The attribute also accepts an optional third argument that determines how the 2268expression is compared to the type tag. There are two supported flags: 2269 2270* ``layout_compatible`` will cause types to be compared according to 2271 layout-compatibility rules (C++11 [class.mem] p 17, 18). This is 2272 implemented to support annotating types like ``MPI_DOUBLE_INT``. 2273 2274 For example: 2275 2276 .. code-block:: c++ 2277 2278 /* In mpi.h */ 2279 struct internal_mpi_double_int { double d; int i; }; 2280 extern struct mpi_datatype mpi_datatype_double_int 2281 __attribute__(( type_tag_for_datatype(mpi, struct internal_mpi_double_int, layout_compatible) )); 2282 2283 #define MPI_DOUBLE_INT ((MPI_Datatype) &mpi_datatype_double_int) 2284 2285 /* In user code */ 2286 struct my_pair { double a; int b; }; 2287 struct my_pair *buffer; 2288 MPI_Send(buffer, 1, MPI_DOUBLE_INT /*, ... */); // no warning 2289 2290 struct my_int_pair { int a; int b; } 2291 struct my_int_pair *buffer2; 2292 MPI_Send(buffer2, 1, MPI_DOUBLE_INT /*, ... */); // warning: actual buffer element 2293 // type 'struct my_int_pair' 2294 // doesn't match specified MPI_Datatype 2295 2296* ``must_be_null`` specifies that the expression should be a null pointer 2297 constant, for example: 2298 2299 .. code-block:: c++ 2300 2301 /* In mpi.h */ 2302 extern struct mpi_datatype mpi_datatype_null 2303 __attribute__(( type_tag_for_datatype(mpi, void, must_be_null) )); 2304 2305 #define MPI_DATATYPE_NULL ((MPI_Datatype) &mpi_datatype_null) 2306 2307 /* In user code */ 2308 MPI_Send(buffer, 1, MPI_DATATYPE_NULL /*, ... */); // warning: MPI_DATATYPE_NULL 2309 // was specified but buffer 2310 // is not a null pointer 2311 2312Format String Checking 2313====================== 2314 2315Clang supports the ``format`` attribute, which indicates that the function 2316accepts a ``printf`` or ``scanf``-like format string and corresponding 2317arguments or a ``va_list`` that contains these arguments. 2318 2319Please see `GCC documentation about format attribute 2320<http://gcc.gnu.org/onlinedocs/gcc/Function-Attributes.html>`_ to find details 2321about attribute syntax. 2322 2323Clang implements two kinds of checks with this attribute. 2324 2325#. Clang checks that the function with the ``format`` attribute is called with 2326 a format string that uses format specifiers that are allowed, and that 2327 arguments match the format string. This is the ``-Wformat`` warning, it is 2328 on by default. 2329 2330#. Clang checks that the format string argument is a literal string. This is 2331 the ``-Wformat-nonliteral`` warning, it is off by default. 2332 2333 Clang implements this mostly the same way as GCC, but there is a difference 2334 for functions that accept a ``va_list`` argument (for example, ``vprintf``). 2335 GCC does not emit ``-Wformat-nonliteral`` warning for calls to such 2336 fuctions. Clang does not warn if the format string comes from a function 2337 parameter, where the function is annotated with a compatible attribute, 2338 otherwise it warns. For example: 2339 2340 .. code-block:: c 2341 2342 __attribute__((__format__ (__scanf__, 1, 3))) 2343 void foo(const char* s, char *buf, ...) { 2344 va_list ap; 2345 va_start(ap, buf); 2346 2347 vprintf(s, ap); // warning: format string is not a string literal 2348 } 2349 2350 In this case we warn because ``s`` contains a format string for a 2351 ``scanf``-like function, but it is passed to a ``printf``-like function. 2352 2353 If the attribute is removed, clang still warns, because the format string is 2354 not a string literal. 2355 2356 Another example: 2357 2358 .. code-block:: c 2359 2360 __attribute__((__format__ (__printf__, 1, 3))) 2361 void foo(const char* s, char *buf, ...) { 2362 va_list ap; 2363 va_start(ap, buf); 2364 2365 vprintf(s, ap); // warning 2366 } 2367 2368 In this case Clang does not warn because the format string ``s`` and 2369 the corresponding arguments are annotated. If the arguments are 2370 incorrect, the caller of ``foo`` will receive a warning. 2371