€•]Q      Œsphinx.addnodes”Œdocument”“”)”}”(Œ	rawsource”Œ ”Œchildren”]”(Œtranslations”ŒLanguagesNode”“”)”}”(hhh]”(h Œpending_xref”“”)”}”(hhh]”Œdocutils.nodes”ŒText”“”ŒChinese (Simplified)”…””}”Œparent”hsbaŒ
attributes”}”(Œids”]”Œclasses”]”Œnames”]”Œdupnames”]”Œbackrefs”]”Œ	refdomain”Œstd”Œreftype”Œdoc”Œ	reftarget”Œ-/translations/zh_CN/arch/arm/kernel_mode_neon”Œmodname”NŒ	classname”NŒrefexplicit”ˆuŒtagname”hhhubh)”}”(hhh]”hŒChinese (Traditional)”…””}”hh2sbah}”(h]”h ]”h"]”h$]”h&]”Œ	refdomain”h)Œreftype”h+Œ	reftarget”Œ-/translations/zh_TW/arch/arm/kernel_mode_neon”Œmodname”NŒ	classname”NŒrefexplicit”ˆuh1hhhubh)”}”(hhh]”hŒItalian”…””}”hhFsbah}”(h]”h ]”h"]”h$]”h&]”Œ	refdomain”h)Œreftype”h+Œ	reftarget”Œ-/translations/it_IT/arch/arm/kernel_mode_neon”Œmodname”NŒ	classname”NŒrefexplicit”ˆuh1hhhubh)”}”(hhh]”hŒJapanese”…””}”hhZsbah}”(h]”h ]”h"]”h$]”h&]”Œ	refdomain”h)Œreftype”h+Œ	reftarget”Œ-/translations/ja_JP/arch/arm/kernel_mode_neon”Œmodname”NŒ	classname”NŒrefexplicit”ˆuh1hhhubh)”}”(hhh]”hŒKorean”…””}”hhnsbah}”(h]”h ]”h"]”h$]”h&]”Œ	refdomain”h)Œreftype”h+Œ	reftarget”Œ-/translations/ko_KR/arch/arm/kernel_mode_neon”Œmodname”NŒ	classname”NŒrefexplicit”ˆuh1hhhubh)”}”(hhh]”hŒSpanish”…””}”hh‚sbah}”(h]”h ]”h"]”h$]”h&]”Œ	refdomain”h)Œreftype”h+Œ	reftarget”Œ-/translations/sp_SP/arch/arm/kernel_mode_neon”Œmodname”NŒ	classname”NŒrefexplicit”ˆuh1hhhubeh}”(h]”h ]”h"]”h$]”h&]”Œcurrent_language”ŒEnglish”uh1h
hhŒ	_document”hŒsource”NŒline”NubhŒsection”“”)”}”(hhh]”(hŒtitle”“”)”}”(hŒKernel mode NEON”h]”hŒKernel mode NEON”…””}”(hh¨hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hh£hžhhŸŒG/var/lib/git/docbuild/linux/Documentation/arch/arm/kernel_mode_neon.rst”h Kubh¢)”}”(hhh]”(h§)”}”(hŒTL;DR summary”h]”hŒTL;DR summary”…””}”(hhºhžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hh·hžhhŸh¶h KubhŒbullet_list”“”)”}”(hhh]”(hŒ	list_item”“”)”}”(hŒOUse only NEON instructions, or VFP instructions that don't rely on support
code”h]”hŒ	paragraph”“”)”}”(hŒOUse only NEON instructions, or VFP instructions that don't rely on support
code”h]”hŒQUse only NEON instructions, or VFP instructions that donâ€™t rely on support
code”…””}”(hhÕhžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h KhhÏubah}”(h]”h ]”h"]”h$]”h&]”uh1hÍhhÊhžhhŸh¶h NubhÎ)”}”(hŒyIsolate your NEON code in a separate compilation unit, and compile it with
'-march=armv7-a -mfpu=neon -mfloat-abi=softfp'”h]”hÔ)”}”(hŒyIsolate your NEON code in a separate compilation unit, and compile it with
'-march=armv7-a -mfpu=neon -mfloat-abi=softfp'”h]”hŒ}Isolate your NEON code in a separate compilation unit, and compile it with
â€˜-march=armv7-a -mfpu=neon -mfloat-abi=softfpâ€™”…””}”(hhíhžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h K	hhéubah}”(h]”h ]”h"]”h$]”h&]”uh1hÍhhÊhžhhŸh¶h NubhÎ)”}”(hŒXPut kernel_neon_begin() and kernel_neon_end() calls around the calls into your
NEON code”h]”hÔ)”}”(hŒXPut kernel_neon_begin() and kernel_neon_end() calls around the calls into your
NEON code”h]”hŒXPut kernel_neon_begin() and kernel_neon_end() calls around the calls into your
NEON code”…””}”(hj  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h Khj  ubah}”(h]”h ]”h"]”h$]”h&]”uh1hÍhhÊhžhhŸh¶h NubhÎ)”}”(hŒ_Don't sleep in your NEON code, and be aware that it will be executed with
preemption disabled

”h]”hÔ)”}”(hŒ]Don't sleep in your NEON code, and be aware that it will be executed with
preemption disabled”h]”hŒ_Donâ€™t sleep in your NEON code, and be aware that it will be executed with
preemption disabled”…””}”(hj  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h Khj  ubah}”(h]”h ]”h"]”h$]”h&]”uh1hÍhhÊhžhhŸh¶h Nubeh}”(h]”h ]”h"]”h$]”h&]”Œbullet”Œ*”uh1hÈhŸh¶h Khh·hžhubeh}”(h]”Œtl-dr-summary”ah ]”h"]”Œtl;dr summary”ah$]”h&]”uh1h¡hh£hžhhŸh¶h Kubh¢)”}”(hhh]”(h§)”}”(hŒIntroduction”h]”hŒIntroduction”…””}”(hjD  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hjA  hžhhŸh¶h KubhÔ)”}”(hX  It is possible to use NEON instructions (and in some cases, VFP instructions) in
code that runs in kernel mode. However, for performance reasons, the NEON/VFP
register file is not preserved and restored at every context switch or taken
exception like the normal register file is, so some manual intervention is
required. Furthermore, special care is required for code that may sleep [i.e.,
may call schedule()], as NEON or VFP instructions will be executed in a
non-preemptible section for reasons outlined below.”h]”hX  It is possible to use NEON instructions (and in some cases, VFP instructions) in
code that runs in kernel mode. However, for performance reasons, the NEON/VFP
register file is not preserved and restored at every context switch or taken
exception like the normal register file is, so some manual intervention is
required. Furthermore, special care is required for code that may sleep [i.e.,
may call schedule()], as NEON or VFP instructions will be executed in a
non-preemptible section for reasons outlined below.”…””}”(hjR  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h KhjA  hžhubeh}”(h]”Œintroduction”ah ]”h"]”Œintroduction”ah$]”h&]”uh1h¡hh£hžhhŸh¶h Kubh¢)”}”(hhh]”(h§)”}”(hŒLazy preserve and restore”h]”hŒLazy preserve and restore”…””}”(hjk  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hjh  hžhhŸh¶h KubhÔ)”}”(hX'  The NEON/VFP register file is managed using lazy preserve (on UP systems) and
lazy restore (on both SMP and UP systems). This means that the register file is
kept 'live', and is only preserved and restored when multiple tasks are
contending for the NEON/VFP unit (or, in the SMP case, when a task migrates to
another core). Lazy restore is implemented by disabling the NEON/VFP unit after
every context switch, resulting in a trap when subsequently a NEON/VFP
instruction is issued, allowing the kernel to step in and perform the restore if
necessary.”h]”hX+  The NEON/VFP register file is managed using lazy preserve (on UP systems) and
lazy restore (on both SMP and UP systems). This means that the register file is
kept â€˜liveâ€™, and is only preserved and restored when multiple tasks are
contending for the NEON/VFP unit (or, in the SMP case, when a task migrates to
another core). Lazy restore is implemented by disabling the NEON/VFP unit after
every context switch, resulting in a trap when subsequently a NEON/VFP
instruction is issued, allowing the kernel to step in and perform the restore if
necessary.”…””}”(hjy  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h Khjh  hžhubhÔ)”}”(hX5  Any use of the NEON/VFP unit in kernel mode should not interfere with this, so
it is required to do an 'eager' preserve of the NEON/VFP register file, and
enable the NEON/VFP unit explicitly so no exceptions are generated on first
subsequent use. This is handled by the function kernel_neon_begin(), which
should be called before any kernel mode NEON or VFP instructions are issued.
Likewise, the NEON/VFP unit should be disabled again after use to make sure user
mode will hit the lazy restore trap upon next use. This is handled by the
function kernel_neon_end().”h]”hX9  Any use of the NEON/VFP unit in kernel mode should not interfere with this, so
it is required to do an â€˜eagerâ€™ preserve of the NEON/VFP register file, and
enable the NEON/VFP unit explicitly so no exceptions are generated on first
subsequent use. This is handled by the function kernel_neon_begin(), which
should be called before any kernel mode NEON or VFP instructions are issued.
Likewise, the NEON/VFP unit should be disabled again after use to make sure user
mode will hit the lazy restore trap upon next use. This is handled by the
function kernel_neon_end().”…””}”(hj‡  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h K'hjh  hžhubeh}”(h]”Œlazy-preserve-and-restore”ah ]”h"]”Œlazy preserve and restore”ah$]”h&]”uh1h¡hh£hžhhŸh¶h Kubh¢)”}”(hhh]”(h§)”}”(hŒInterruptions in kernel mode”h]”hŒInterruptions in kernel mode”…””}”(hj   hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hj  hžhhŸh¶h K2ubhÔ)”}”(hX  For reasons of performance and simplicity, it was decided that there shall be no
preserve/restore mechanism for the kernel mode NEON/VFP register contents. This
implies that interruptions of a kernel mode NEON section can only be allowed if
they are guaranteed not to touch the NEON/VFP registers. For this reason, the
following rules and restrictions apply in the kernel:
* NEON/VFP code is not allowed in interrupt context;
* NEON/VFP code is not allowed to sleep;
* NEON/VFP code is executed with preemption disabled.”h]”hX  For reasons of performance and simplicity, it was decided that there shall be no
preserve/restore mechanism for the kernel mode NEON/VFP register contents. This
implies that interruptions of a kernel mode NEON section can only be allowed if
they are guaranteed not to touch the NEON/VFP registers. For this reason, the
following rules and restrictions apply in the kernel:
* NEON/VFP code is not allowed in interrupt context;
* NEON/VFP code is not allowed to sleep;
* NEON/VFP code is executed with preemption disabled.”…””}”(hj®  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h K3hj  hžhubhÔ)”}”(hX#  If latency is a concern, it is possible to put back to back calls to
kernel_neon_end() and kernel_neon_begin() in places in your code where none of
the NEON registers are live. (Additional calls to kernel_neon_begin() should be
reasonably cheap if no context switch occurred in the meantime)”h]”hX#  If latency is a concern, it is possible to put back to back calls to
kernel_neon_end() and kernel_neon_begin() in places in your code where none of
the NEON registers are live. (Additional calls to kernel_neon_begin() should be
reasonably cheap if no context switch occurred in the meantime)”…””}”(hj¼  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h K<hj  hžhubeh}”(h]”Œinterruptions-in-kernel-mode”ah ]”h"]”Œinterruptions in kernel mode”ah$]”h&]”uh1h¡hh£hžhhŸh¶h K2ubh¢)”}”(hhh]”(h§)”}”(hŒVFP and support code”h]”hŒVFP and support code”…””}”(hjÕ  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hjÒ  hžhhŸh¶h KCubhÔ)”}”(hXˆ  Earlier versions of VFP (prior to version 3) rely on software support for things
like IEEE-754 compliant underflow handling etc. When the VFP unit needs such
software assistance, it signals the kernel by raising an undefined instruction
exception. The kernel responds by inspecting the VFP control registers and the
current instruction and arguments, and emulates the instruction in software.”h]”hXˆ  Earlier versions of VFP (prior to version 3) rely on software support for things
like IEEE-754 compliant underflow handling etc. When the VFP unit needs such
software assistance, it signals the kernel by raising an undefined instruction
exception. The kernel responds by inspecting the VFP control registers and the
current instruction and arguments, and emulates the instruction in software.”…””}”(hjã  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h KDhjÒ  hžhubhÔ)”}”(hŒ²Such software assistance is currently not implemented for VFP instructions
executed in kernel mode. If such a condition is encountered, the kernel will
fail and generate an OOPS.”h]”hŒ²Such software assistance is currently not implemented for VFP instructions
executed in kernel mode. If such a condition is encountered, the kernel will
fail and generate an OOPS.”…””}”(hjñ  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h KJhjÒ  hžhubeh}”(h]”Œvfp-and-support-code”ah ]”h"]”Œvfp and support code”ah$]”h&]”uh1h¡hh£hžhhŸh¶h KCubh¢)”}”(hhh]”(h§)”}”(hŒ'Separating NEON code from ordinary code”h]”hŒ'Separating NEON code from ordinary code”…””}”(hj
  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hj  hžhhŸh¶h KPubhÔ)”}”(hXÔ  The compiler is not aware of the special significance of kernel_neon_begin() and
kernel_neon_end(), i.e., that it is only allowed to issue NEON/VFP instructions
between calls to these respective functions. Furthermore, GCC may generate NEON
instructions of its own at -O3 level if -mfpu=neon is selected, and even if the
kernel is currently compiled at -O2, future changes may result in NEON/VFP
instructions appearing in unexpected places if no special care is taken.”h]”hXÔ  The compiler is not aware of the special significance of kernel_neon_begin() and
kernel_neon_end(), i.e., that it is only allowed to issue NEON/VFP instructions
between calls to these respective functions. Furthermore, GCC may generate NEON
instructions of its own at -O3 level if -mfpu=neon is selected, and even if the
kernel is currently compiled at -O2, future changes may result in NEON/VFP
instructions appearing in unexpected places if no special care is taken.”…””}”(hj  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h KQhj  hžhubhÔ)”}”(hŒxTherefore, the recommended and only supported way of using NEON/VFP in the
kernel is by adhering to the following rules:”h]”hŒxTherefore, the recommended and only supported way of using NEON/VFP in the
kernel is by adhering to the following rules:”…””}”(hj&  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h KXhj  hžhubhÉ)”}”(hhh]”(hÎ)”}”(hŒxisolate the NEON code in a separate compilation unit and compile it with
'-march=armv7-a -mfpu=neon -mfloat-abi=softfp';”h]”hÔ)”}”(hŒxisolate the NEON code in a separate compilation unit and compile it with
'-march=armv7-a -mfpu=neon -mfloat-abi=softfp';”h]”hŒ|isolate the NEON code in a separate compilation unit and compile it with
â€˜-march=armv7-a -mfpu=neon -mfloat-abi=softfpâ€™;”…””}”(hj;  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h K[hj7  ubah}”(h]”h ]”h"]”h$]”h&]”uh1hÍhj4  hžhhŸh¶h NubhÎ)”}”(hŒÇissue the calls to kernel_neon_begin(), kernel_neon_end() as well as the calls
into the unit containing the NEON code from a compilation unit which is *not*
built with the GCC flag '-mfpu=neon' set.
”h]”hÔ)”}”(hŒÆissue the calls to kernel_neon_begin(), kernel_neon_end() as well as the calls
into the unit containing the NEON code from a compilation unit which is *not*
built with the GCC flag '-mfpu=neon' set.”h]”(hŒ—issue the calls to kernel_neon_begin(), kernel_neon_end() as well as the calls
into the unit containing the NEON code from a compilation unit which is ”…””}”(hjS  hžhhŸNh NubhŒemphasis”“”)”}”(hŒ*not*”h]”hŒnot”…””}”(hj]  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1j[  hjS  ubhŒ.
built with the GCC flag â€˜-mfpu=neonâ€™ set.”…””}”(hjS  hžhhŸNh Nubeh}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h K]hjO  ubah}”(h]”h ]”h"]”h$]”h&]”uh1hÍhj4  hžhhŸh¶h Nubeh}”(h]”h ]”h"]”h$]”h&]”j7  j8  uh1hÈhŸh¶h K[hj  hžhubhÔ)”}”(hŒ¼As the kernel is compiled with '-msoft-float', the above will guarantee that
both NEON and VFP instructions will only ever appear in designated compilation
units at any optimization level.”h]”hŒÀAs the kernel is compiled with â€˜-msoft-floatâ€™, the above will guarantee that
both NEON and VFP instructions will only ever appear in designated compilation
units at any optimization level.”…””}”(hj  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h Kahj  hžhubeh}”(h]”Œ'separating-neon-code-from-ordinary-code”ah ]”h"]”Œ'separating neon code from ordinary code”ah$]”h&]”uh1h¡hh£hžhhŸh¶h KPubh¢)”}”(hhh]”(h§)”}”(hŒNEON assembler”h]”hŒNEON assembler”…””}”(hjš  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hj—  hžhhŸh¶h KgubhÔ)”}”(hŒ_NEON assembler is supported with no additional caveats as long as the rules
above are followed.”h]”hŒ_NEON assembler is supported with no additional caveats as long as the rules
above are followed.”…””}”(hj¨  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h Khhj—  hžhubeh}”(h]”Œneon-assembler”ah ]”h"]”Œneon assembler”ah$]”h&]”uh1h¡hh£hžhhŸh¶h Kgubh¢)”}”(hhh]”(h§)”}”(hŒNEON code generated by GCC”h]”hŒNEON code generated by GCC”…””}”(hjÁ  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hj¾  hžhhŸh¶h KmubhÔ)”}”(hŒÍThe GCC option -ftree-vectorize (implied by -O3) tries to exploit implicit
parallelism, and generates NEON code from ordinary C source code. This is fully
supported as long as the rules above are followed.”h]”hŒÍThe GCC option -ftree-vectorize (implied by -O3) tries to exploit implicit
parallelism, and generates NEON code from ordinary C source code. This is fully
supported as long as the rules above are followed.”…””}”(hjÏ  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h Knhj¾  hžhubeh}”(h]”Œneon-code-generated-by-gcc”ah ]”h"]”Œneon code generated by gcc”ah$]”h&]”uh1h¡hh£hžhhŸh¶h Kmubh¢)”}”(hhh]”(h§)”}”(hŒNEON intrinsics”h]”hŒNEON intrinsics”…””}”(hjè  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1h¦hjå  hžhhŸh¶h KtubhÔ)”}”(hŒÐNEON intrinsics are also supported. However, as code using NEON intrinsics
relies on the GCC header <arm_neon.h>, (which #includes <stdint.h>), you should
observe the following in addition to the rules above:”h]”hŒÐNEON intrinsics are also supported. However, as code using NEON intrinsics
relies on the GCC header <arm_neon.h>, (which #includes <stdint.h>), you should
observe the following in addition to the rules above:”…””}”(hjö  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h Kuhjå  hžhubhÉ)”}”(hhh]”(hÎ)”}”(hŒ¬Compile the unit containing the NEON intrinsics with '-ffreestanding' so GCC
uses its builtin version of <stdint.h> (this is a C99 header which the kernel
does not supply);”h]”hÔ)”}”(hŒ¬Compile the unit containing the NEON intrinsics with '-ffreestanding' so GCC
uses its builtin version of <stdint.h> (this is a C99 header which the kernel
does not supply);”h]”hŒ°Compile the unit containing the NEON intrinsics with â€˜-ffreestandingâ€™ so GCC
uses its builtin version of <stdint.h> (this is a C99 header which the kernel
does not supply);”…””}”(hj  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h Kyhj  ubah}”(h]”h ]”h"]”h$]”h&]”uh1hÍhj  hžhhŸh¶h NubhÎ)”}”(hŒ<Include <arm_neon.h> last, or at least after <linux/types.h>”h]”hÔ)”}”(hj!  h]”hŒ<Include <arm_neon.h> last, or at least after <linux/types.h>”…””}”(hj#  hžhhŸNh Nubah}”(h]”h ]”h"]”h$]”h&]”uh1hÓhŸh¶h K|hj  ubah}”(h]”h ]”h"]”h$]”h&]”uh1hÍhj  hžhhŸh¶h Nubeh}”(h]”h ]”h"]”h$]”h&]”j7  j8  uh1hÈhŸh¶h Kyhjå  hžhubeh}”(h]”Œneon-intrinsics”ah ]”h"]”Œneon intrinsics”ah$]”h&]”uh1h¡hh£hžhhŸh¶h Ktubeh}”(h]”Œkernel-mode-neon”ah ]”h"]”Œkernel mode neon”ah$]”h&]”uh1h¡hhhžhhŸh¶h Kubeh}”(h]”h ]”h"]”h$]”h&]”Œsource”h¶uh1hŒcurrent_source”NŒcurrent_line”NŒsettings”Œdocutils.frontend”ŒValues”“”)”}”(h¦NŒ	generator”NŒ	datestamp”NŒsource_link”NŒ
source_url”NŒtoc_backlinks”Œentry”Œfootnote_backlinks”KŒsectnum_xform”KŒstrip_comments”NŒstrip_elements_with_classes”NŒstrip_classes”NŒreport_level”KŒ
halt_level”KŒexit_status_level”KŒdebug”NŒwarning_stream”NŒ	traceback”ˆŒinput_encoding”Œ	utf-8-sig”Œinput_encoding_error_handler”Œstrict”Œoutput_encoding”Œutf-8”Œoutput_encoding_error_handler”jo  Œerror_encoding”Œutf-8”Œerror_encoding_error_handler”Œbackslashreplace”Œlanguage_code”Œen”Œrecord_dependencies”NŒconfig”NŒ	id_prefix”hŒauto_id_prefix”Œid”Œdump_settings”NŒdump_internals”NŒdump_transforms”NŒdump_pseudo_xml”NŒexpose_internals”NŒstrict_visitor”NŒ_disable_config”NŒ_source”h¶Œ_destination”NŒ_config_files”]”Œ7/var/lib/git/docbuild/linux/Documentation/docutils.conf”aŒfile_insertion_enabled”ˆŒraw_enabled”KŒline_length_limit”M'Œpep_references”NŒpep_base_url”Œhttps://peps.python.org/”Œpep_file_url_template”Œpep-%04d”Œrfc_references”NŒrfc_base_url”Œ&https://datatracker.ietf.org/doc/html/”Œ	tab_width”KŒtrim_footnote_reference_space”‰Œsyntax_highlight”Œlong”Œsmart_quotes”ˆŒsmartquotes_locales”]”Œcharacter_level_inline_markup”‰Œdoctitle_xform”‰Œdocinfo_xform”KŒsectsubtitle_xform”‰Œimage_loading”Œlink”Œembed_stylesheet”‰Œcloak_email_addresses”ˆŒsection_self_link”‰Œenv”NubŒreporter”NŒindirect_targets”]”Œsubstitution_defs”}”Œsubstitution_names”}”Œrefnames”}”Œrefids”}”Œnameids”}”(jI  jF  j>  j;  je  jb  jš  j—  jÏ  jÌ  j  j  j”  j‘  j»  j¸  jâ  jß  jA  j>  uŒ	nametypes”}”(jI  ‰j>  ‰je  ‰jš  ‰jÏ  ‰j  ‰j”  ‰j»  ‰jâ  ‰jA  ‰uh}”(jF  h£j;  h·jb  jA  j—  jh  jÌ  j  j  jÒ  j‘  j  j¸  j—  jß  j¾  j>  jå  uŒfootnote_refs”}”Œcitation_refs”}”Œautofootnotes”]”Œautofootnote_refs”]”Œsymbol_footnotes”]”Œsymbol_footnote_refs”]”Œ	footnotes”]”Œ	citations”]”Œautofootnote_start”KŒsymbol_footnote_start”K Œ
id_counter”Œcollections”ŒCounter”“”}”…”R”Œparse_messages”]”Œtransform_messages”]”Œtransformer”NŒinclude_log”]”Œ
decoration”Nhžhub.