Commit Graph

231730 Commits

Author SHA1 Message Date
christos c94539ae6b handle the "special" wc NULL case. 2014-11-15 17:49:19 +00:00
uebayasi 017bd8df74 LINKSCRIPT is set only once, so use = not +=. 2014-11-15 15:01:41 +00:00
jmcneill 645822f2c8 enable awinir, cir 2014-11-15 14:59:25 +00:00
jmcneill 9be0a63059 add A20 IR support 2014-11-15 14:56:18 +00:00
uebayasi 98b59f518b Use LINKSCRIPT. 2014-11-15 14:55:02 +00:00
uebayasi b7590d7122 Use LINKSCRIPT. 2014-11-15 14:25:10 +00:00
uebayasi e49865688b Use LINKSCRIPT. 2014-11-15 14:02:19 +00:00
uebayasi 7c8e115825 Use LINKSCRIPT. 2014-11-15 13:41:16 +00:00
jmcneill 6d4a77d1ce hide a debug printf 2014-11-15 13:41:11 +00:00
jmcneill bd4dbfad29 Fix CIR setup. Works on A31 now. 2014-11-15 13:40:39 +00:00
uebayasi d4908ddcd5 Use LINKSCRIPT. 2014-11-15 13:34:30 +00:00
uebayasi 2bdcfe8a70 Stop ordering dependencies alphabetically. 2014-11-15 12:56:28 +00:00
uebayasi 104daad189 Use LINKSCRIPT. 2014-11-15 12:36:42 +00:00
uebayasi 15151b11c7 Bump image size from 512MB to 520MB. 2014-11-15 12:33:04 +00:00
uebayasi 634cfde5a0 Use LINKSCRIPT. 2014-11-15 12:20:06 +00:00
uebayasi dfd51da465 config(1): Avoid buffer overrun (modular build) 2014-11-15 12:18:55 +00:00
uebayasi 70dd8e7d2a config(1): Sort objects by weight in modular build
Sort per-module kernel objects (*.ko) by dependency weight.  Important modules
are placed in lower addresses.  The ``machdep'' module will be always placed
in the lowest.

(At this moment, the order is not exact because dependency information is
incomplete in config files (files.*).  Thus ``sysmon_power.ko'' comes lower
than ``machdep.ko'' and/or ``uvm.ko''; but still much better than alphabetical
sort.)
2014-11-15 08:21:38 +00:00
uebayasi 1a322b21d7 Don't sort objects for modular build. 2014-11-15 08:20:42 +00:00
uebayasi fdd72c8f74 Separate linker script argument (${LINKSCRIPT}) from ${LINKFORMAT}
${LINKFORMAT} specifies ABI options, and used for ld -r.  ${LINKSCRIPT} (-T
ldscript) is used only for final link.
2014-11-15 08:20:01 +00:00
tsutsui 1d361e78b9 Expand heap to 64KB so that bootxx can load bootxxx from 32KB blocksize ffs.
Tested on TT030 with 32GB SSD via SATA->IDE->SCSI converters.
Should be pulled up to netbsd-7 and netbsd-6 branches..
2014-11-15 06:30:10 +00:00
manu 620512b8f3 Fix UFS1 extended attribute backend autocreation deadlock
UFS1 extended attribute backend autocration goes through a vn_open()
to create the backend file, and this forces us to release the lock
on the target node, in case the target is within the parents of the
backend file. That created a window within which another thread could
acquire a lock on the target vnode and deadlock awaiting for the
mount extended attribute lock.

We fix the problem by also releasing the mount extended attribute lock
when calling vn_open(), but that lets another thread race us for backend
creation. We just detect this using O_EXCL for vn_open() and by checking
for EEXIST return code. If we are raced, we fail backend creation but
this is not a problem since another thread succeeded on it: we just have
to use the result.
2014-11-15 05:03:55 +00:00
uebayasi ef5efd2fc9 Tweaks. 2014-11-15 04:47:11 +00:00
uebayasi 03a2e2df43 Test object reordering by script. 2014-11-15 04:23:48 +00:00
uebayasi 551b230b22 Test object ordering. 2014-11-15 03:47:29 +00:00
uebayasi b57644333c Merge tests. 2014-11-15 03:22:29 +00:00
uebayasi e6ae210ca4 Tweak. 2014-11-15 03:10:01 +00:00
joerg 7c080d8b84 Show display if it is not empty. 2014-11-15 02:09:18 +00:00
joerg 84c8bd741e Array can't be null. 2014-11-15 02:01:27 +00:00
joerg 0bab8dfecf Use l_wmesg if the string is not empty. Don't bother checking l_name for
nullness.
2014-11-15 01:58:34 +00:00
joerg c87c6690c0 Skip vendor if the string is empty. 2014-11-15 01:52:01 +00:00
joerg 755f404f87 Remove tautologic check. 2014-11-15 01:24:53 +00:00
joerg f7673b99b4 Comment out impossible code. 2014-11-15 01:24:38 +00:00
joerg 31a77d8abb Drop pointer checks that are always true. 2014-11-15 01:15:45 +00:00
jmcneill 8820e4401c Implement WSDISPLAYIO_SVIDEO, WSDISPLAYIO_GVIDEO for screen blanking 2014-11-14 23:45:02 +00:00
wiz 57a81568cf bump year 2014-11-14 22:46:34 +00:00
jmcneill a2af6ae803 Allow the DEBE layer and output sizes to be set independently. Now you can
pass fb.margin=<n> in bootargs to add a border to the framebuffer, in case
your display doesn't let you turn off overscan and you really want to see
the whole screen.
2014-11-14 19:47:36 +00:00
maxv 833172a8e0 Do not uselessly include <sys/malloc.h>. 2014-11-14 17:34:23 +00:00
riastradh 995f5ce060 Commit to returning 1, not any nonzero value. 2014-11-14 16:43:57 +00:00
uebayasi 29c8a787f1 Tweak previous. 2014-11-14 16:29:03 +00:00
uebayasi e0d81d86b9 Test orphan ELF section placement. 2014-11-14 16:21:12 +00:00
uebayasi 1fc7d1e960 Fix thinko in previous. 2014-11-14 16:20:42 +00:00
joerg 5e9c3bb2be Install cpuid.h on X86 and arm_neon.h on ARM. 2014-11-14 15:59:46 +00:00
joerg f26a5b846f LLVM switched to three component point release version, so follow here. 2014-11-14 15:56:12 +00:00
joerg f88c0f1c84 Define copysignl on !long double platforms. Be consistent in the use of
weak aliases.
2014-11-14 14:53:17 +00:00
oster e222077349 Adjust comment to reflect reality. (5th arg, not 4th) 2014-11-14 14:45:34 +00:00
joerg 930df7c121 Fix build with clang. 2014-11-14 14:32:49 +00:00
oster 404e5f061e Fix a long-standing bug related to rebooting while a
reconstruct-to-spare is underway but not yet complete.

The issue was that a component was being marked as a used_spare when
the rebuild started, not when the rebuild was actually finished.
Marking it as a used_spare meant that the component label on the spare
was being updated such that after a reboot the component would be
considered up-to-date, regardless of whether the rebuild actually
completed!

This fix includes:
 1) Add an additional state "rf_ds_rebuilding_spare" which is used
    to denote that a spare is currently being rebuilt from the live
    components.
 2) Update the comments on the disk states, which were out-of-sync
    with reality.
 3) When rebuilding to a spare component, that spare now enters the
    state rf_ds_rebuilding_spare instead of the state rf_ds_used_spare.
 4) When the rebuild is actually complete then the spare component
    enters the rf_ds_used_spare state.  rf_ds_used_spare is now used
    exclusively for the case where the rebuilding to the spare has
    completed successfully.

XXX: Someday we need to teach raidctl(8) about this new state, and
take out the backwards compatibility code in rf_netbsdkintf.c (see
RAIDFRAME_GET_INFO in raidioctl()).  For today, this fix needs to be
generic enough that it can get backported without major grief.

XXX: Needs pullup to netbsd-5*, netbsd-6*, and netbsd-7

Fixes PR#49244.
2014-11-14 14:29:16 +00:00
uebayasi 90e9fce862 Test __start_xxx/__stop_xxx symbol generation. 2014-11-14 13:30:48 +00:00
roy e4d839ca92 Note import of dhcpcd-6.6.2 2014-11-14 12:02:20 +00:00
roy 3c322f3bc1 Sync 2014-11-14 12:00:54 +00:00